[UR][L0] urBindlessImagesGetImageMemoryHandleTypeSupportExp correction (#19667)

VK_FORMAT_R8G8B8A8_UNORM is supported on L0 urt, correction to
verifyCommonImagePropertiesSupport.

---------

Signed-off-by: Zhang, Winston <[email protected]>

Author: winstonzhang-intel

sycl/test-e2e/bindless_images/dx11_interop/read_write_unsampled.cpp

@@ -213,7 +213,10 @@ int runTest(D3D11ProgramState &d3d11ProgramState, sycl::queue syclQueue,
   // E.g. LevelZero does not support `unorm` channel types.
   if (!bindless_helpers::memoryAllocationSupported(
           syclImageDesc, syclexp::image_memory_handle_type::opaque_handle,
-          syclQueue)) {
+          syclQueue) ||
+      (channelType == sycl::image_channel_type::unorm_int8 &&
+       syclQueue.get_device().get_backend() ==
+           sycl::backend::ext_oneapi_level_zero)) {
     // We cannot allocate the image memory, skip the test.
 #ifdef VERBOSE_PRINT
     std::cout << "Memory allocation unsupported. Skipping test.\n";

sycl/test-e2e/bindless_images/dx12_interop/read_write_unsampled.cpp

@@ -523,6 +523,14 @@ static bool
 runTest(DX12SYCLDevice &device, sycl::image_channel_type channelType,
         sycl::range<NDims> globalSize, sycl::range<NDims> localSize) {
 
+  // Skip unorm_int8 tests for Level Zero backend
+  if (channelType == sycl::image_channel_type::unorm_int8 &&
+      device.getSyclQueue().get_device().get_backend() ==
+          sycl::backend::ext_oneapi_level_zero) {
+    std::cout << "Skipping unorm_int8 test for Level Zero backend.\n";
+    return true;
+  }
+
   syclexp::image_descriptor syclImageDesc{globalSize, NChannels, channelType};
 
   // Verify ability to allocate the above image descriptor.

unified-runtime/source/adapters/level_zero/image_common.cpp

@@ -1016,16 +1016,6 @@ bool verifyCommonImagePropertiesSupport(
     }
   }
 
-  // Verify unnormalized channel type support.
-  // LevelZero currently doesn't support unnormalized channel types.
-  switch (pImageFormat->channelType) {
-  default:
-    break;
-  case UR_IMAGE_CHANNEL_TYPE_UNORM_INT8:
-  case UR_IMAGE_CHANNEL_TYPE_UNORM_INT16:
-    return false;
-  }
-
   return supported;
 }