CUDA Academy · บทเรียน

เงื่อนไขแข่งขันบน GPU

ทำไมการเขียนพร้อมกันจึงทำให้ข้อมูลเสียหาย

บทเรียน 1 จาก 413 ขั้นตอน

เงื่อนไขแข่งขันบน 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 ในทันที — ไม่ต้องติดตั้งในเครื่องของคุณ

บทเรียนทั้งหมดในหลักสูตรนี้

  1. เงื่อนไขแข่งขันบน GPU
  2. atomicAdd และฟังก์ชันที่เกี่ยวข้อง
  3. สร้างฮิสโตแกรม
  4. การดำเนินการอะตอมิกแบบกำหนดเองด้วย atomicCAS
← กลับไปที่ CUDA Academy