From f911bdf3b5bfe793ad04df5a62e425d3ed5508b5 Mon Sep 17 00:00:00 2001
From: PSuchita <31720043+PSuchita@users.noreply.github.com>
Date: Fri, 15 Mar 2019 15:43:48 -0500
Subject: Update cudaStreamDestroy function

Update cudaStreamDestroy's functionality to synchronize before destroying streams.
---
 libcuda/cuda_runtime_api.cc | 1 +
 1 file changed, 1 insertion(+)

diff --git a/libcuda/cuda_runtime_api.cc b/libcuda/cuda_runtime_api.cc
index 27644b3..3ff3212 100644
--- a/libcuda/cuda_runtime_api.cc
+++ b/libcuda/cuda_runtime_api.cc
@@ -1569,6 +1569,7 @@ __host__ cudaError_t CUDARTAPI cudaStreamDestroy(cudaStream_t stream)
 	    announce_call(__my_func__);
     }
 #if (CUDART_VERSION >= 3000)
+	synchronize();
 	g_stream_manager->destroy_stream(stream);
 #endif
 	return g_last_cudaError = cudaSuccess;
-- 
cgit v1.3


From 981c79b0f3e1c637755bfa8dd0b2dbac1d44a865 Mon Sep 17 00:00:00 2001
From: PSuchita <31720043+PSuchita@users.noreply.github.com>
Date: Fri, 15 Mar 2019 16:26:28 -0500
Subject: Added comment

Adding comment to describe the issue resolved by the previous commit related to cudaStreamDestroy.
---
 libcuda/cuda_runtime_api.cc | 1 +
 1 file changed, 1 insertion(+)

diff --git a/libcuda/cuda_runtime_api.cc b/libcuda/cuda_runtime_api.cc
index 3ff3212..920be46 100644
--- a/libcuda/cuda_runtime_api.cc
+++ b/libcuda/cuda_runtime_api.cc
@@ -1569,6 +1569,7 @@ __host__ cudaError_t CUDARTAPI cudaStreamDestroy(cudaStream_t stream)
 	    announce_call(__my_func__);
     }
 #if (CUDART_VERSION >= 3000)
+	//synchronization required to avoid the stream_manager from spinning forever to destroy non-empty streams without making any forward progress.
 	synchronize();
 	g_stream_manager->destroy_stream(stream);
 #endif
-- 
cgit v1.3


From d575f9464df6358d1be60953e984bcfa9257d1a3 Mon Sep 17 00:00:00 2001
From: PSuchita <31720043+PSuchita@users.noreply.github.com>
Date: Fri, 15 Mar 2019 17:13:16 -0500
Subject: Updated comment.

---
 libcuda/cuda_runtime_api.cc | 3 ++-
 1 file changed, 2 insertions(+), 1 deletion(-)

diff --git a/libcuda/cuda_runtime_api.cc b/libcuda/cuda_runtime_api.cc
index 920be46..cf16d9b 100644
--- a/libcuda/cuda_runtime_api.cc
+++ b/libcuda/cuda_runtime_api.cc
@@ -1569,7 +1569,8 @@ __host__ cudaError_t CUDARTAPI cudaStreamDestroy(cudaStream_t stream)
 	    announce_call(__my_func__);
     }
 #if (CUDART_VERSION >= 3000)
-	//synchronization required to avoid the stream_manager from spinning forever to destroy non-empty streams without making any forward progress.
+	//synchronization required for application using external libraries without explicit synchronization in the code to 
+	//avoid the stream_manager from spinning forever to destroy non-empty streams without making any forward progress. 
 	synchronize();
 	g_stream_manager->destroy_stream(stream);
 #endif
-- 
cgit v1.3