add as_hal for Queue

Cargo.toml

@@ -54,7 +54,7 @@ keywords = ["graphics"]
 license = "MIT OR Apache-2.0"
 homepage = "https://wgpu.rs/"
 repository = "https://github.com/gfx-rs/wgpu"
-version = "24.0.0"
+version = "24.0.1"
 authors = ["gfx-rs developers"]
 
 [workspace.dependencies]

wgpu-hal/src/metal/mod.rs

@@ -356,6 +356,10 @@ impl Queue {
             timestamp_period,
         }
     }
+
+    pub fn as_raw(&self) -> parking_lot::MutexGuard<'_, metal::CommandQueue> {
+        self.raw.lock()
+    }
 }
 
 pub struct Device {

wgpu/src/api/queue.rs

@@ -251,4 +251,26 @@ impl Queue {
     pub fn on_submitted_work_done(&self, callback: impl FnOnce() + Send + 'static) {
         self.inner.on_submitted_work_done(Box::new(callback));
     }
+
+    /// Returns the inner hal Queue using a callback. The hal queue will be `None` if the
+    /// backend type argument does not match with this wgpu Queue
+    ///
+    /// # Safety
+    ///
+    /// - The raw handle obtained from the hal Queue must not be manually destroyed
+    #[cfg(wgpu_core)]
+    pub unsafe fn as_hal<A: wgc::hal_api::HalApi, F: FnOnce(Option<&A::Queue>) -> R, R>(
+        &self,
+        hal_queue_callback: F,
+    ) -> R {
+        if let Some(core_queue) = self.inner.as_core_opt() {
+            unsafe {
+                core_queue
+                    .context
+                    .queue_as_hal::<A, F, R>(core_queue, hal_queue_callback)
+            }
+        } else {
+            hal_queue_callback(None)
+        }
+    }
 }

wgpu/src/backend/wgpu_core.rs

@@ -360,6 +360,14 @@ impl ContextWgpuCore {
 
         format!("Validation Error\n\nCaused by:\n{output}")
     }
+
+    pub unsafe fn queue_as_hal<A: wgc::hal_api::HalApi, F: FnOnce(Option<&A::Queue>) -> R, R>(
+        &self,
+        queue: &CoreQueue,
+        hal_queue_callback: F,
+    ) -> R {
+        unsafe { self.0.queue_as_hal::<A, F, R>(queue.id, hal_queue_callback) }
+    }
 }
 
 fn map_buffer_copy_view(view: crate::TexelCopyBufferInfo<'_>) -> wgc::command::TexelCopyBufferInfo {