test

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

Author: winstonzhang-intel

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

@@ -1,9 +1,4 @@
-// REQUIRES: aspect-ext_oneapi_external_memory_import
-// REQUIRES: windows
 
-// UNSUPPORTED: gpu-intel-gen12
-// UNSUPPORTED-INTENDED: Unknown issue with integrated GPU failing
-//                       when importing memory
 
 // RUN: %{build} %link-directx -o %t.out
 // RUN: %{run-unfiltered-devices} env NEOReadDebugKeys=1 UseBindlessMode=1 UseExternalAllocatorForSshAndDsh=1 %t.out
@@ -248,25 +243,31 @@ int runTest(D3D11ProgramState &d3d11ProgramState, sycl::queue syclQueue,
   // it is only applicable to 2D textures.
   texDesc.MiscFlags = D3D11_RESOURCE_MISC_SHARED_NTHANDLE |
                       D3D11_RESOURCE_MISC_SHARED_KEYEDMUTEX;
+  printf("1\n");
   ThrowIfFailed(pDevice->CreateTexture2D(&texDesc, nullptr, &texture));
 
   // Create the keyed mutex for synchronising the shared resource.
   ComPtr<IDXGIKeyedMutex> keyedMutex;
+  printf("2\n");
   ThrowIfFailed(texture.As(&keyedMutex));
   d3d11ProgramState.key = 0;
 
   // Create an NT handle to a shared resource referring to our texture.
   // Opening the shared resource gives access to it for use on the SYCL device.
   ComPtr<IDXGIResource1> sharedResource;
+  printf("3\n");
   ThrowIfFailed(texture.As(&sharedResource));
   HANDLE sharedHandle = nullptr;
+  printf("4\n");
   ThrowIfFailed(sharedResource->CreateSharedHandle(
       nullptr, DXGI_SHARED_RESOURCE_READ | DXGI_SHARED_RESOURCE_WRITE, nullptr,
       &sharedHandle));
 
   // Obtain a pointer to the shared resource for use in subsequent operations.
   ComPtr<ID3D11Device1> device1;
+  printf("5\n");
   ThrowIfFailed(pDevice->QueryInterface(IID_PPV_ARGS(&device1)));
+  printf("6\n");
   ThrowIfFailed(device1->OpenSharedResource1(
       sharedHandle, IID_PPV_ARGS(sharedResource.GetAddressOf())));
 
@@ -300,10 +301,12 @@ int runTest(D3D11ProgramState &d3d11ProgramState, sycl::queue syclQueue,
   // When IDXGIKeyedMutex importing into SYCL is implemented, we'll be able to
   // call it from the SYCL API. All it does is ensuring only one device has
   // exclusive access.
+  printf("7\n");
   ThrowIfFailed(keyedMutex->AcquireSync(d3d11ProgramState.key++, INFINITE));
   callSyclKernel<NDims, DType, NChannels>(syclQueue, syclImageHandle,
                                           globalSize, localSize);
   // Back to the D3D11 process
+  printf("8\n");
   ThrowIfFailed(keyedMutex->ReleaseSync(d3d11ProgramState.key));
 
   // Read-back and verify