[SYCL][Bindless] Fix get_image_num_channels failing with mipmap images (#15036)

This patch fixes a crash due to get_image_num_channels expecting a
CUarray instead of a CUmipmappedArray. Expands test coverage to test
this.

Author: DBDuncan

sycl/cmake/modules/FetchUnifiedRuntime.cmake

@@ -117,13 +117,13 @@ if(SYCL_UR_USE_FETCH_CONTENT)
   endfunction()
 
   set(UNIFIED_RUNTIME_REPO "https://github.com/oneapi-src/unified-runtime.git")
-  # commit b4195cbb694b6e7c6216bf42a757ed700a325855
-  # Merge: 5482621c ab77d020
+  # commit 76361a88a0af6502fe655144655b381260ea9706
+  # Merge: b4195cb 0db57da
   # Author: Omar Ahmed <[email protected]>
-  # Date:   Mon Aug 26 14:00:04 2024 +0100
-  #    Merge pull request #2006 from zhaomaosu/devsan-fix-cxxlib-mismatch
-  #    [DeviceSanitizer] Fix libstdc++ and libc++ mismatch problem
-  set(UNIFIED_RUNTIME_TAG b4195cbb694b6e7c6216bf42a757ed700a325855)
+  # Date:   Wed, 31 Jul 2024 14:26:38 +0100
+  #    Merge pull request #1961 from DBDuncan/duncan/num-channels-mipmap-fix 
+  #    [Bindless][Exp] Fix urBindlessImagesImageGetInfoExp failing with mipmap images
+  set(UNIFIED_RUNTIME_TAG 76361a88a0af6502fe655144655b381260ea9706)
 
   set(UMF_BUILD_EXAMPLES OFF CACHE INTERNAL "EXAMPLES")
   # Due to the use of dependentloadflag and no installer for UMF and hwloc we need

sycl/test-e2e/bindless_images/image_get_info.cpp

@@ -229,6 +229,31 @@ int main() {
       validated = false;
     }
 
+    // Extension: image descriptor -- number of levels
+    sycl::ext::oneapi::experimental::image_descriptor mipDesc(
+        {width, height}, 4, sycl::image_channel_type::signed_int32,
+        sycl::ext::oneapi::experimental::image_type::mipmap, 3);
+
+    // Extension: allocate mipmap memory on device
+    sycl::ext::oneapi::experimental::image_mem mipMem(mipDesc, q);
+
+    auto numChannelsMipMem = mipMem.get_num_channels();
+    auto numChannelsMip =
+        sycl::ext::oneapi::experimental::get_image_num_channels(
+            mipMem.get_handle(), dev, ctxt);
+
+    if (numChannelsMipMem != numChannelsMip) {
+      printString(
+          "mipmap handle and mem object disagree on number of channels!\n");
+      validated = false;
+    }
+    if (numChannelsMip == 4) {
+      printString("mipmap num channels is correct!\n");
+    } else {
+      printString("mipmap num channels is NOT correct!\n");
+      validated = false;
+    }
+
   } catch (sycl::exception e) {
     std::cerr << "SYCL exception caught! : " << e.what() << "\n";
     return 1;