✨🚧 Support DX11 on textures without copy (see #2 (comment))

Author: davidAlgis

Plugin/PluginInteropUnityCUDA/src/Buffer/vertex_buffer_D3D11.cpp

@@ -7,7 +7,9 @@
 
 VertexBuffer_D3D11::VertexBuffer_D3D11(void* bufferHandle, int size)
 	: VertexBuffer(bufferHandle, size)
-{}
+{
+	Log::log().debugLogError("Vertex buffer interoperability on DX11 is not yet supported");
+}
 
 VertexBuffer_D3D11::~VertexBuffer_D3D11()
 {
@@ -20,14 +22,16 @@ VertexBuffer_D3D11::~VertexBuffer_D3D11()
 /// </summary>
 void VertexBuffer_D3D11::registerBufferInCUDA()
 {
-	Log::log().debugLog("try register");
+
+	Log::log().debugLogError("Register buffer on DX11 is not yet supported");
 	// register the texture to cuda : it initialize the _pGraphicsResource
-	CUDA_CHECK(cudaGraphicsD3D11RegisterResource(&_pGraphicsResource, (ID3D11Resource*)_bufferHandle, cudaGraphicsRegisterFlagsWriteDiscard));
-	Log::log().debugLog("register");}
+	// CUDA_CHECK(cudaGraphicsD3D11RegisterResource(&_pGraphicsResource, (ID3D11Resource*)_bufferHandle, cudaGraphicsRegisterFlagsWriteDiscard));
+}
 
 void VertexBuffer_D3D11::unRegisterBufferInCUDA()
 {
-	CUDA_CHECK(cudaGraphicsUnregisterResource(_pGraphicsResource));
+	Log::log().debugLogError("Unregister buffer on DX11 is not yet supported");
+	// CUDA_CHECK(cudaGraphicsUnregisterResource(_pGraphicsResource));
 }
 
 

Plugin/PluginInteropUnityCUDA/src/Texture/texture_D3D11.cpp

@@ -16,7 +16,7 @@ Texture_D3D11::Texture_D3D11(void *textureHandle, int textureWidth,
 
 Texture_D3D11::~Texture_D3D11()
 {
-    _texBufferInterop->Release();
+    // _texBufferInterop->Release();
     CUDA_CHECK(cudaGetLastError());
 };
 
@@ -28,33 +28,31 @@ Texture_D3D11::~Texture_D3D11()
 void Texture_D3D11::registerTextureInCUDA()
 {
 
-    // This method initialize the buffer textures that will be registered in
-    // CUDA This method will use m_device attributes in RenderAPI_D3D11, make
-    // sure it has been well initialized.
-    int retCodeCreate = _renderAPI->createTexture2D(
-        _textureWidth, _textureHeight, _textureDepth, &_texBufferInterop);
-    // we initialize
-    if (retCodeCreate < 0)
+    // we cast it here, to make it only once.
+    if(_textureDepth < 1)
     {
-        Log::log().debugLogError("Could not initialize texture on DX11 for "
-                                 "copy. Interoperability has failed.");
+        auto texUnityDX11 = (ID3D11Texture2D *)_textureHandle;
+        CUDA_CHECK(cudaGraphicsD3D11RegisterResource(
+                &_pGraphicsResource, texUnityDX11, cudaGraphicsRegisterFlagsNone));
+        CUDA_CHECK(cudaGetLastError());
     }
-
-
-    // we cast it here, to make it only once.
-    _texUnityDX11 = (ID3D11Texture2D *)_textureHandle;
-    // assert(_texBufferInterop);
+    else
+    {
+        auto texUnityDX11 = (ID3D11Texture3D *)_textureHandle;
+        CUDA_CHECK(cudaGraphicsD3D11RegisterResource(
+                &_pGraphicsResource, texUnityDX11, cudaGraphicsRegisterFlagsNone));
+        CUDA_CHECK(cudaGetLastError());
+    }
+    // assert(texUnityDX11);
     // D3D11_TEXTURE2D_DESC texDesc;
-    // _texBufferInterop->GetDesc(&texDesc);
+    // texUnityDX11->GetDesc(&texDesc);
 
     // DXGI_FORMAT format = texDesc.Format;
     // Log::log().debugLog(std::to_string(format));
 
     // CUDA_CHECK(cudaGetLastError());
     // register the texture to cuda : it initialize the _pGraphicsResource
-    CUDA_CHECK(cudaGraphicsD3D11RegisterResource(
-        &_pGraphicsResource, _texBufferInterop, cudaGraphicsRegisterFlagsNone));
-    CUDA_CHECK(cudaGetLastError());
+    
 }
 
 void Texture_D3D11::unRegisterTextureInCUDA()

Plugin/SampleBasic/src/action_sample_texture.cpp

@@ -31,9 +31,7 @@ int ActionSampleTexture::Update()
     kernelCallerWriteTexture(_texture->getDimGrid(), _texture->getDimBlock(),
                              _surf, GetTime(), _texture->getWidth(),
                              _texture->getHeight());
-    cudaDeviceSynchronize();
-    // Log::log().debugLog("copy from API to Unity");
-    _texture->copyAPITextureToUnityTexture();
+    // cudaDeviceSynchronize();
     return 0;
 }