เงื่อนไขแข่งขันบน GPU
ทำไมการเขียนพร้อมกันจึงทำให้ข้อมูลเสียหาย
เงื่อนไขแข่งขันบน GPU เป็นบทเรียน CUDA Academy ฟรีบน CoddyKit นี่คือบทเรียนที่ 1 จากทั้งหมด 4 บทเรียน คุณสามารถอ่านบทเรียนทั้งหมดด้านล่างฟรี — จากนั้นลองปฏิบัติด้วยตัวคุณเองในเบราว์เซอร์พร้อมตัวแก้ไขโค้ดในตัวและติวเตอร์ AI ตลอด 24/7 บทเรียนนี้เป็นส่วนหนึ่งของเส้นทางการเรียน CUDA Academy และความก้าวหน้าของคุณจะซิงค์ข้ามเว็บและแอป CoddyKit คอร์ส CUDA Academy มีบทเรียนทั้งหมด 4 บทเรียน
หลายมือ เคาน์เตอร์เดียว
บน GPU เธรดหลายพันเธรดสามารถเข้าถึงหน่วยความจำเดียวกันได้พร้อมกัน เมื่อหลายเธรดเขียนไปยังตำแหน่งเดียวกันพร้อมกัน จะเกิด สภาวะแข่งขัน 🏁
สภาวะแข่งขันคืออะไร
สภาวะแข่งขันเกิดขึ้นเมื่อผลลัพธ์สุดท้ายขึ้นอยู่กับลำดับการทำงานของเธรดที่คาดเดาไม่ได้ โค้ดเดียวกันอาจให้คำตอบต่างกันในการเรียกใช้แต่ละครั้ง
อ่าน-แก้ไข-เขียน
การเพิ่มค่าเคาน์เตอร์จริง ๆ แล้วมีสามขั้นตอน ได้แก่ อ่านค่า เพิ่มหนึ่ง และเขียนค่ากลับ ลำดับ อ่าน-แก้ไข-เขียนนี้คือจุดที่ปัญหาเกิดขึ้น
counter = counter + 1;ขั้นตอนเหลื่อมล้ำกันอย่างไร
เธรดสองเธรดอ่านค่า 5 พร้อมกัน คำนวณได้ 6 พร้อมกัน และเขียนค่า 6 พร้อมกัน คุณคาดว่าจะได้ 7 แต่กลับได้ 6 การเพิ่มค่าครั้งหนึ่งหายไปโดยไม่มีสัญญาณเตือน
การปรับปรุงที่หายไป
การเพิ่มค่าที่หายไปนี้เรียกว่า การปรับปรุงที่สูญหาย เมื่อมีเธรดหลายพันเธรดแข่งขันกัน การปรับปรุงหลายสิบหรือหลายร้อยรายการอาจหายไปพร้อมกัน
เคอร์เนลที่ดูถูกต้อง
เคอร์เนลนี้ดูถูกต้อง แต่เธรดทุกเธรดกำลังแข่งขันกันเข้าถึงแอดเดรสเดียวกัน จำนวนสุดท้ายจะผิดและ เปลี่ยนแปลงไปมา ในการเรียกใช้แต่ละครั้ง
__global__ void count(int* total) {
*total = *total + 1;
}เหตุใดผลลัพธ์จึงไม่กำหนดแน่นอน
ฮาร์ดแวร์ไม่เคยรับประกันลำดับของเธรด ดังนั้นเคอร์เนลที่มีสภาวะแข่งขันจึงให้ผลลัพธ์แบบ ไม่กำหนดแน่นอน และอาจผ่านการทดสอบกับอินพุตขนาดเล็ก แต่ล้มเหลวกับอินพุตขนาดใหญ่
การอ่านเพียงอย่างเดียวปลอดภัย
การที่หลายเธรด อ่านค่าเดียวกันถือว่าปลอดภัยอย่างสมบูรณ์ ปัญหาจะเริ่มขึ้นเมื่อมีเธรดอย่างน้อยหนึ่งเธรดเขียนค่า ขณะที่เธรดอื่นอ่านหรือเขียน
การเขียนคนละตำแหน่งก็ปลอดภัยเช่นกัน
หากแต่ละเธรดเขียนลงช่องเฉพาะของตนเอง เช่น out[i] จะไม่มีความขัดแย้ง สภาวะแข่งขันจะเกิดขึ้นก็ต่อเมื่อเธรดมุ่งไปยังตำแหน่งเดียวกัน
out[i] = a[i] + b[i];ตัวอย่างวิธีแก้
วิธีแก้คือทำให้การอ่าน-แก้ไข-เขียนเกิดขึ้นเป็นขั้นตอนเดียวที่แบ่งแยกไม่ได้ นั่นคือการดำเนินการแบบ อะตอมิก ซึ่งจะอธิบายในบทถัดไป ⚛️
ตรวจหาสภาวะแข่งขันระหว่างการตรวจทาน
เมื่อตรวจทานเคอร์เนล ให้ถามว่าเธรดสองเธรดเขียนลงแอดเดรสเดียวกันโดยไม่มีการป้องกันหรือไม่ หากใช่ คุณแทบจะแน่ใจได้ว่ามี สภาวะแข่งขันของข้อมูล
ตรวจสอบความเข้าใจอย่างรวดเร็ว
มาดูกันว่าแนวคิดเรื่องสภาวะแข่งขันชัดเจนแล้วหรือยัง
สรุป: สภาวะแข่งขันบน GPU
คุณได้เรียนรู้ว่าการอ่าน-แก้ไข-เขียนข้อมูลใช้ร่วมกันโดยไม่มีการป้องกันทำให้เกิด สภาวะแข่งขันและการปรับปรุงที่สูญหาย บทถัดไปคืออะตอมิก ซึ่งทำให้ขั้นตอนเหล่านั้นแบ่งแยกไม่ได้ ✅
เรียนรู้ C++ ด้วย AI tutor — ฟรี
เขียนและเรียกใช้โค้ดจริงในเบราว์เซอร์ของคุณ รับความช่วยเหลือทันทีจาก AI tutor 24/7 และเรียนรู้ต่อจากที่คุณหยุดบนเว็บหรือในแอป
- คอร์ส
- 30
- บทเรียน
- 120
คำถามที่พบบ่อย
บทเรียน “เงื่อนไขแข่งขันบน GPU” ฟรีหรือไม่
ใช่ — ข้อความเต็มของ “เงื่อนไขแข่งขันบน GPU” ฟรีให้อ่านที่นี่บนเว็บ เพื่อปฏิบัติแบบโต้ตอบ (ตัวแก้ไขโค้ดในตัวและติวเตอร์ AI ตลอด 24/7) และปลดล็อคส่วนที่เหลือของคอร์ส CUDA Academy ให้อัปเกรดเป็น CoddyKit PRO คอร์ส CUDA Academy มีบทเรียนทั้งหมด 4 บทเรียน
คุณจะเรียนรู้อะไรในบทเรียน “เงื่อนไขแข่งขันบน GPU”
ทำไมการเขียนพร้อมกันจึงทำให้ข้อมูลเสียหาย คุณปฏิบัติ CUDA Academy ด้วยโค้ดที่ใช้งานได้จริงที่คุณเรียกใช้โดยตรงในเบราว์เซอร์ และติวเตอร์ AI ตลอด 24/7 ตอบคำถามของคุณขณะที่คุณไปผ่านบทเรียน
คุณต้องมีประสบการณ์ก่อนที่จะเริ่มเรียน CUDA Academy หรือไม่
ไม่จำเป็นต้องมีประสบการณ์มาก่อน CUDA Academy บน CoddyKit ออกแบบมาสำหรับผู้เริ่มต้นไปจนถึงผู้เรียนขั้นสูง คุณสามารถเริ่มต้นที่นี่หรือเริ่มจากตัวแรกและเรียนด้วยความเร็วของคุณเอง นี่คือบทเรียนที่ 1 จากทั้งหมด 4 บทเรียน
บทเรียน “เงื่อนไขแข่งขันบน GPU” ใช้เวลานานแค่ไหน
บทเรียน CoddyKit ส่วนใหญ่ใช้เวลาประมาณ 5–10 นาที แต่ละบทเรียนจึงสั้นและเป็นแบบโต้ตอบ คุณสามารถก้าวหน้าอย่างต่อเนื่องและกลับมาเรียนต่อจากตรงที่เพิ่งหยุดบนเว็บและแอปได้เลย
ฉันเขียนและรันโค้ดในบทเรียน CUDA Academy นี้ได้ไหม
ได้ บทเรียน CUDA Academy ทุกบทมีตัวแก้ไขโค้ดในตัว คุณจึงเขียนและรันโค้ดจริงได้เลยในเบราว์เซอร์ และได้รับข้อเสนอแนะจาก AI ในทันที — ไม่ต้องติดตั้งในเครื่องของคุณ
บทเรียนทั้งหมดในหลักสูตรนี้
- เงื่อนไขแข่งขันบน GPU
- atomicAdd และฟังก์ชันที่เกี่ยวข้อง
- สร้างฮิสโตแกรม
- การดำเนินการอะตอมิกแบบกำหนดเองด้วย atomicCAS