diff --git a/sycl/test-e2e/bindless_images/dx11_interop/read_write_unsampled.cpp b/sycl/test-e2e/bindless_images/dx11_interop/read_write_unsampled.cpp index 1d97f1b386ebb..5d2f1226adfce 100644 --- a/sycl/test-e2e/bindless_images/dx11_interop/read_write_unsampled.cpp +++ b/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"; diff --git a/sycl/test-e2e/bindless_images/dx12_interop/read_write_unsampled.cpp b/sycl/test-e2e/bindless_images/dx12_interop/read_write_unsampled.cpp index 6a8a3fd8c2285..b318af5ebe17d 100644 --- a/sycl/test-e2e/bindless_images/dx12_interop/read_write_unsampled.cpp +++ b/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 globalSize, sycl::range 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. diff --git a/unified-runtime/source/adapters/level_zero/image_common.cpp b/unified-runtime/source/adapters/level_zero/image_common.cpp index 531a270e9fdc5..10f2ef1430ce2 100644 --- a/unified-runtime/source/adapters/level_zero/image_common.cpp +++ b/unified-runtime/source/adapters/level_zero/image_common.cpp @@ -1014,16 +1014,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; }