דף זה תורגם על ידי Cloud Translation API.

מה חדש ב-WebGPU (Chrome123)

François Beaufort

תמיכה בפונקציות מובנות של DP4a ב-WGSL

‫DP4a (Dot Product of 4 Elements and Accumulate) מתייחס לקבוצה של הוראות GPU שנמצאות בשימוש נפוץ בהסקת מסקנות של למידה עמוקה לצורך קוונטיזציה. הוא מבצע ביעילות מכפלות סקלריות של מספרים שלמים בני 8 ביט כדי להאיץ את החישוב של מודלים כאלה שעברו קוונטיזציה של int8. הוא יכול לחסוך (עד 75%) בזיכרון וברוחב הפס של הרשת, ולשפר את הביצועים של כל מודל למידת מכונה בהסקת מסקנות בהשוואה לגרסת f32 שלו. כתוצאה מכך, נעשה בו שימוש נרחב בהרבה מסגרות AI פופולריות.

אם "packed_4x8_integer_dot_product" WGSL language extension קיים ב-navigator.gpu.wgslLanguageFeatures, עכשיו אפשר להשתמש בסקלרים של מספרים שלמים בני 32 ביט לאריזת וקטורים של 4 רכיבים של מספרים שלמים בני 8 ביט כקלט להוראות של מכפלה סקלרית בקוד של הצללה ב-WGSL באמצעות הפונקציות המובנות dot4U8Packed ו-dot4I8Packed. אפשר גם להשתמש בהוראות אריזה ופריקה עם וקטורים ארוזים של 4 רכיבים של מספרים שלמים בני 8 ביט עם הפונקציות המובנות של WGSL‏: pack4xI8,‏ pack4xU8,‏ pack4xI8Clamp,‏ pack4xU8Clamp,‏ unpack4xI8 ו-unpack4xU8.

מומלץ להשתמש בrequires-directive כדי לציין את האפשרות לאי-ניידות באמצעות requires packed_4x8_integer_dot_product; בחלק העליון של קוד ה-shader של WGSL. אפשר לעיין בדוגמה הבאה ובבעיה מספר tint:1497.

if (!navigator.gpu.wgslLanguageFeatures.has("packed_4x8_integer_dot_product")) {
  throw new Error(`DP4a built-in functions are not available`);
}

const adapter = await navigator.gpu.requestAdapter();
const device = await adapter.requestDevice();

const shaderModule = device.createShaderModule({ code: `
  requires packed_4x8_integer_dot_product;

  fn main() {
    const result: u32 = dot4U8Packed(0x01020304u, 0x02040405u); // 42
  }`,
});

תודה מיוחדת לצוות הגרפיקה באינטרנט של Intel בשנגחאי על קידום המפרט וההטמעה עד להשלמה!

פרמטרים של מצביעים ללא הגבלה ב-WGSL

"unrestricted_pointer_parameters" תוסף השפה "unrestricted_pointer_parameters" WGSL "unrestricted_pointer_parameters"מבטל את ההגבלות על המצביעים שאפשר להעביר לפונקציות WGSL:

מצביעי פרמטרים של מרחבי הכתובות storage, uniform ו-workgroup לפונקציות שהמשתמש הצהיר עליהן.
העברת מצביעים לחברי מבנה ולאלמנטים של מערך לפונקציות שהמשתמש הצהיר עליהן.

מידע נוסף זמין במאמר Pointers As Function Parameters | Tour of WGSL.

אפשר לזהות את התכונה הזו באמצעות navigator.gpu.wgslLanguageFeatures. מומלץ להשתמש תמיד בrequires-directive כדי לציין את האפשרות לאי-ניידות באמצעות requires unrestricted_pointer_parameters; בחלק העליון של קוד ה-shader של WGSL. אפשר לעיין בדוגמה הבאה, בשינויים במפרט של WGSL ובבעיה tint:2053.

if (!navigator.gpu.wgslLanguageFeatures.has("unrestricted_pointer_parameters")) {
  throw new Error(`Unrestricted pointer parameters are not available`);
}

const adapter = await navigator.gpu.requestAdapter();
const device = await adapter.requestDevice();

const shaderModule = device.createShaderModule({ code: `
  requires unrestricted_pointer_parameters;

  @group(0) @binding(0) var<storage, read_write> S : i32;

  fn func(pointer : ptr<storage, i32, read_write>) {
    *pointer = 42;
  }

  @compute @workgroup_size(1)
  fn main() {
    func(&S);
  }`
});

תהליך הוספה של סוכר תחבירי לביטול ההפניה למרכיבים ב-WGSL

אם "pointer_composite_access" התוסף לשפת WGSL מופיע ב-navigator.gpu.wgslLanguageFeatures, קוד ה-shader של WGSL תומך עכשיו בגישה לרכיבים של סוגי נתונים מורכבים באמצעות אותו תחביר של נקודה (.), בין אם אתם עובדים ישירות עם הנתונים או עם מצביע לנתונים. ככה זה עובד:

אם foo הוא מצביע: foo.bar היא דרך נוחה יותר לכתוב (*foo).bar. בדרך כלל צריך להוסיף כוכבית (*) כדי להפוך את המצביע ל'הפניה' שאפשר לבטל את ההפניה שלה, אבל עכשיו המצביעים וההפניות דומים הרבה יותר ואפשר להשתמש בהם לסירוגין.
אם foo הוא לא מצביע: האופרטור של הנקודה (.) פועל בדיוק כמו שאתם רגילים לגישה ישירה למשתנים.

באופן דומה, אם pa הוא מצביע שמאחסן את כתובת ההתחלה של מערך, השימוש ב-pa[i] מאפשר גישה ישירה למיקום בזיכרון שבו מאוחסן הרכיב ה-'i של המערך הזה.

מומלץ להשתמש בrequires-directive כדי לציין את האפשרות לאי-ניידות באמצעות requires pointer_composite_access; בחלק העליון של קוד ה-shader של WGSL. אפשר לעיין בדוגמה הבאה ובבעיה tint:2113.

if (!navigator.gpu.wgslLanguageFeatures.has("pointer_composite_access")) {
  throw new Error(`Pointer composite access is not available`);
}

const adapter = await navigator.gpu.requestAdapter();
const device = await adapter.requestDevice();

const shaderModule = device.createShaderModule({ code: `
  requires pointer_composite_access;

  fn main() {
    var a = vec3f();
    let p : ptr<function, vec3f> = &a;
    let r1 = (*p).x; // always valid.
    let r2 = p.x; // requires pointer composite access.
  }`
});

מצב נפרד של קריאה בלבד לאספקטים של סטנסיל ועומק

בעבר, קבצים מצורפים של סטנסיל עומק לקריאה בלבד במעברי רינדור דרשו ששני ההיבטים (עומק וסטנסיל) יהיו לקריאה בלבד. המגבלה הזו הוסרה. עכשיו אפשר להשתמש בהיבט העומק במצב קריאה בלבד, למשל למעקב אחרי צללים של אנשי קשר, בזמן שמאגר הסטנסיל נכתב כדי לזהות פיקסלים לעיבוד נוסף. מידע נוסף

עדכונים של Dawn

הקריאה החוזרת (callback) של שגיאה שלא נתפסה שהוגדרה באמצעות wgpuDeviceSetUncapturedErrorCallback() נקראת עכשיו באופן מיידי כשהשגיאה מתרחשת. זה מה שמפתחים מצפים לו באופן עקבי ורוצים לניפוי באגים. מידע נוסף

השיטה wgpuSurfaceGetPreferredFormat() מ-webgpu.h API הוטמעה. מידע נוסף

המידע הזה כולל רק נקודות עיקריות. רשימה מלאה של קומיטים