ตัวระบุคุณสมบัติฟังก์ชัน __global__
กำหนดให้ฟังก์ชันเป็นเคอร์เนลของ GPU
ตัวระบุคุณสมบัติฟังก์ชัน __global__ เป็นบทเรียน CUDA Academy ฟรีบน CoddyKit นี่คือบทเรียนที่ 1 จากทั้งหมด 4 บทเรียน คุณสามารถอ่านบทเรียนทั้งหมดด้านล่างฟรี — จากนั้นลองปฏิบัติด้วยตัวคุณเองในเบราว์เซอร์พร้อมตัวแก้ไขโค้ดในตัวและติวเตอร์ AI ตลอด 24/7 บทเรียนนี้เป็นส่วนหนึ่งของเส้นทางการเรียน CUDA Academy และความก้าวหน้าของคุณจะซิงค์ข้ามเว็บและแอป CoddyKit คอร์ส CUDA Academy มีบทเรียนทั้งหมด 4 บทเรียน
สองโลก สองคอมไพเลอร์
ไฟล์ CUDA ของคุณมีทั้งโค้ด CPU และ GPU คำสำคัญเล็ก ๆ จะบอกคอมไพเลอร์ว่าฟังก์ชันนั้นอยู่ฝั่งใด คำสำคัญนั้นคือ ตัวระบุฟังก์ชัน ⚡
ทำความรู้จัก __global__
ตัวระบุ __global__ กำหนดฟังก์ชันให้เป็นเคอร์เนล GPU ซึ่ง CPU เป็นผู้เรียกใช้ แต่ GPU เป็นผู้ทำงานผ่านเธรดจำนวนมาก
__global__ void myKernel() {
// runs on the GPU
}เรียกที่นี่ ทำงานที่นั่น
ฟังก์ชัน __global__ เป็นชนิดเดียวที่โฮสต์เรียกได้ แต่อุปกรณ์เป็นผู้ทำงาน ฟังก์ชันนี้คือสะพานเชื่อมระหว่างสองโลกของคุณ
คืนค่าเป็น void เสมอ
เคอร์เนลต้องคืนค่าเป็น void ไม่สามารถส่งค่ากลับไปยัง CPU ได้ ดังนั้นผลลัพธ์จึงต้องส่งออกผ่านหน่วยความจำแทน
__global__ void addOne(int* data) {
data[0] += 1;
}การเรียกใช้งานเป็นแบบอะซิงโครนัส
เมื่อคุณเรียกใช้เคอร์เนล __global__ CPU จะไม่รอ การเรียกจะคืนค่าทันทีขณะที่ GPU ทำงานอยู่เบื้องหลัง 🚀
หลายเธรด ฟังก์ชันเดียว
นิยาม __global__ เดียวสามารถทำงานบนเธรดหลายพันเธรดพร้อมกัน คุณเขียนเนื้อหาฟังก์ชันเพียงครั้งเดียว แล้ว GPU จะทำงานนั้นซ้ำไปยังแกนประมวลผลต่าง ๆ
รูปแบบการเรียกใช้งาน
การเรียกใช้เคอร์เนลต้องใช้ วงเล็บมุมสามชั้นแบบพิเศษเพื่อกำหนดจำนวนเธรดที่จะทำงาน การใช้วงเล็บกลมปกติเพียงอย่างเดียวไม่เพียงพอ
myKernel<<<1, 256>>>();พารามิเตอร์แบบส่งค่า
อาร์กิวเมนต์ของเคอร์เนลจะถูกคัดลอกไปยังอุปกรณ์ สำหรับอาร์เรย์ให้ส่ง ตัวชี้ไปยังหน่วยความจำอุปกรณ์ เพราะตัวชี้ของโฮสต์ไม่มีความหมายบน GPU
ไม่เหมือนกับ __device__
อย่าสับสนระหว่างสองสิ่งนี้: __global__ คือจุดเริ่มต้นที่เรียกใช้งานได้ ส่วนฟังก์ชัน __device__ เป็นฟังก์ชันช่วยที่เรียกได้จากโค้ด GPU เท่านั้น
ไม่มีการเรียกซ้ำที่จุดเริ่มต้น
เคอร์เนล __global__ ไม่สามารถเรียกตัวเองโดยตรงแบบฟังก์ชันโฮสต์ได้ การเรียกซ้ำแบบดั้งเดิมควรอยู่ในฟังก์ชันช่วยของอุปกรณ์แทน
เหตุผลที่เรื่องนี้สำคัญ
การเชี่ยวชาญ __global__ จะเปิดทางไปสู่ทุกเรื่องถัดไป: ทุกเคอร์เนลที่คุณเขียน เรียกใช้ และปรับแต่ง ล้วนเริ่มต้นจากคำสำคัญเล็ก ๆ นี้
ตรวจสอบอย่างรวดเร็ว
มาทดสอบความเข้าใจของคุณเกี่ยวกับตัวระบุ __global__ กัน
สรุปทบทวน
คุณได้เรียนรู้ว่า __global__ ใช้กำหนดเคอร์เนล GPU: โฮสต์เป็นผู้เรียก อุปกรณ์เป็นผู้ทำงาน คืนค่าเป็น void และเรียกใช้ด้วยวงเล็บมุมสามชั้น 🎉
คำถามที่พบบ่อย
บทเรียน “ตัวระบุคุณสมบัติฟังก์ชัน __global__” ฟรีหรือไม่
ใช่ — ข้อความเต็มของ “ตัวระบุคุณสมบัติฟังก์ชัน __global__” ฟรีให้อ่านที่นี่บนเว็บ เพื่อปฏิบัติแบบโต้ตอบ (ตัวแก้ไขโค้ดในตัวและติวเตอร์ AI ตลอด 24/7) และปลดล็อคส่วนที่เหลือของคอร์ส CUDA Academy ให้อัปเกรดเป็น CoddyKit PRO คอร์ส CUDA Academy มีบทเรียนทั้งหมด 4 บทเรียน
คุณจะเรียนรู้อะไรในบทเรียน “ตัวระบุคุณสมบัติฟังก์ชัน __global__”
กำหนดให้ฟังก์ชันเป็นเคอร์เนลของ GPU คุณปฏิบัติ CUDA Academy ด้วยโค้ดที่ใช้งานได้จริงที่คุณเรียกใช้โดยตรงในเบราว์เซอร์ และติวเตอร์ AI ตลอด 24/7 ตอบคำถามของคุณขณะที่คุณไปผ่านบทเรียน
คุณต้องมีประสบการณ์ก่อนที่จะเริ่มเรียน CUDA Academy หรือไม่
ไม่จำเป็นต้องมีประสบการณ์มาก่อน CUDA Academy บน CoddyKit ออกแบบมาสำหรับผู้เริ่มต้นไปจนถึงผู้เรียนขั้นสูง คุณสามารถเริ่มต้นที่นี่หรือเริ่มจากตัวแรกและเรียนด้วยความเร็วของคุณเอง นี่คือบทเรียนที่ 1 จากทั้งหมด 4 บทเรียน
บทเรียน “ตัวระบุคุณสมบัติฟังก์ชัน __global__” ใช้เวลานานแค่ไหน
บทเรียน CoddyKit ส่วนใหญ่ใช้เวลาประมาณ 5–10 นาที แต่ละบทเรียนจึงสั้นและเป็นแบบโต้ตอบ คุณสามารถก้าวหน้าอย่างต่อเนื่องและกลับมาเรียนต่อจากตรงที่เพิ่งหยุดบนเว็บและแอปได้เลย
ฉันเขียนและรันโค้ดในบทเรียน CUDA Academy นี้ได้ไหม
ได้ บทเรียน CUDA Academy ทุกบทมีตัวแก้ไขโค้ดในตัว คุณจึงเขียนและรันโค้ดจริงได้เลยในเบราว์เซอร์ และได้รับข้อเสนอแนะจาก AI ในทันที — ไม่ต้องติดตั้งในเครื่องของคุณ
บทเรียนทั้งหมดในหลักสูตรนี้
- ตัวระบุคุณสมบัติฟังก์ชัน __global__
- ฟังก์ชัน __device__ และ __host__
- พื้นที่แอดเดรสแยกจากกัน
- วงจรชีวิตของโปรแกรม CUDA