Implement bindless buffers on metal

CHANGELOG.md

@@ -173,6 +173,8 @@ By @stuartparmenter in [#9658](https://github.com/gfx-rs/wgpu/pull/9658).
 - Add `metal::Queue::add_wait_event` / `add_signal_event` (with `remove_*` companions) to stage `MTLSharedEvent` waits/signals on the next `Queue::submit`, for GPU-side interop with foreign APIs. Waits run on an internal CB committed before user CBs. By @AdrianEddy in [#9483](https://github.com/gfx-rs/wgpu/pull/9483).
 - Unconditionally enable `Features::CLIP_DISTANCES`. By @ErichDonGubler in [#9270](https://github.com/gfx-rs/wgpu/pull/9270).
 - Added full support for mesh shaders, including in WGSL shaders. By @inner-daemons in [#8739](https://github.com/gfx-rs/wgpu/pull/8739).
+- Fixed structure field names incorrectly ignoring reserved keywords in the Metal (MSL) backend. By @39ali [#9379](https://github.com/gfx-rs/wgpu/pull/9379).
+- Added support for bindless storage buffers (buffer binding arrays) on Metal. By @mate-h in [#9081](https://github.com/gfx-rs/wgpu/pull/9081).
 - Added `DropCallback`s to Metal textures. By @jerzywilczek in [#9634](https://github.com/gfx-rs/wgpu/pull/9634).
 
 #### GLES

naga/src/back/msl/mod.rs

@@ -424,6 +424,39 @@ pub struct PipelineOptions {
     /// vertex_buffer_mappings are used during shader translation to
     /// support vertex pulling.
     pub vertex_buffer_mappings: Vec<VertexBufferMapping>,
+
+    /// For each storage `binding_array` in the pipeline layout, the number of
+    /// elements that layout declares, keyed by `ResourceBinding`.
+    /// The MSL writer uses this to report the number of elements in an unbounded `binding_array`.
+    #[cfg_attr(
+        feature = "deserialize",
+        serde(deserialize_with = "deserialize_binding_array_length_map")
+    )]
+    pub binding_array_length_map: crate::FastHashMap<crate::ResourceBinding, u32>,
+}
+
+#[cfg(feature = "deserialize")]
+#[derive(serde::Deserialize)]
+struct BindingArrayLengthMapSerialization {
+    resource_binding: crate::ResourceBinding,
+    count: u32,
+}
+
+#[cfg(feature = "deserialize")]
+fn deserialize_binding_array_length_map<'de, D>(
+    deserializer: D,
+) -> Result<crate::FastHashMap<crate::ResourceBinding, u32>, D::Error>
+where
+    D: serde::Deserializer<'de>,
+{
+    use serde::Deserialize;
+
+    let vec = Vec::<BindingArrayLengthMapSerialization>::deserialize(deserializer)?;
+    let mut map = crate::FastHashMap::default();
+    for item in vec {
+        map.insert(item.resource_binding, item.count);
+    }
+    Ok(map)
 }
 
 impl Options {