Fixed leak

Author: nyalloc

sycl/plugins/cuda/pi_cuda.cpp

@@ -2811,11 +2811,6 @@ pi_result cuda_piextEventCreateWithNativeHandle(pi_native_handle nativeHandle,
   return {};
 }
 
-_pi_sampler::_pi_sampler(pi_context context) {
-  context_ = context;
-  props_ = 0;
-}
-
 /// Creates a PI sampler object
 ///
 /// \param[in] context The context the sampler is created for.
@@ -2940,7 +2935,7 @@ pi_result cuda_piSamplerRelease(pi_sampler sampler) {
   // double delete or someone is messing with the ref count.
   // either way, cannot safely proceed.
   cl::sycl::detail::pi::assertion(
-      sampler->get_reference_count() > 0,
+      sampler->get_reference_count() != 0,
       "Reference count overflow detected in cuda_piSamplerRelease.");
 
   // decrement ref count. If it is 0, delete the sampler.

sycl/plugins/cuda/pi_cuda.hpp

@@ -581,7 +581,8 @@ struct _pi_sampler {
   pi_uint32 props_;
   pi_context context_;
 
-  _pi_sampler(pi_context context);
+  _pi_sampler(pi_context context)
+      : refCount_(1), props_(0), context_(context) {}
 
   pi_uint32 increment_reference_count() noexcept { return ++refCount_; }