Unify event implementation

include/ghex/device/cuda/event.hpp

@@ -27,8 +27,8 @@ struct cuda_event
     cudaEvent_t           m_event;
     ghex::util::moved_bit m_moved;
 
-    cuda_event() {
-        GHEX_CHECK_CUDA_RESULT(cudaEventCreateWithFlags(&m_event, cudaEventDisableTiming))
+    cuda_event(unsigned int flags = cudaEventDisableTiming) {
+        GHEX_CHECK_CUDA_RESULT(cudaEventCreateWithFlags(&m_event, flags))
     };
     cuda_event(const cuda_event&) = delete;
     cuda_event& operator=(const cuda_event&) = delete;
@@ -40,15 +40,7 @@ struct cuda_event
         if (!m_moved) { GHEX_CHECK_CUDA_RESULT_NO_THROW(cudaEventDestroy(m_event)) }
     }
 
-    /**
-     * @brief	Returns `true` if `*this` has been moved, i.e. can no longer be used.
-     *
-     * @todo  The semantic of this function is a bit confusing as a valid object returns
-     *   `false`. It should be changed such that a valid object returns `true` and an
-     *   invalid one returns `false`. This is the behaviour for `GHEX_C_STRUCT` and
-     *   `GHEX_C_MANAGED_STRUCT` but not for `stream` and `cuda_event`.
-     */
-    operator bool() const noexcept { return m_moved; }
+    operator bool() const noexcept { return !m_moved; }
 
     cudaEvent_t& get() noexcept
     {
@@ -60,6 +52,9 @@ struct cuda_event
         assert(!m_moved);
         return m_event;
     }
+
+    operator cudaEvent_t&() noexcept { return get(); }
+    operator const cudaEvent_t&() const noexcept { return get(); }
 };
 } // namespace device
 } // namespace ghex

include/ghex/device/cuda/event_pool.hpp

@@ -70,7 +70,7 @@ struct event_pool
         while (!(m_next_event < m_events.size())) { m_events.emplace_back(cuda_event()); }
 
         const std::size_t event_to_use = m_next_event;
-        assert(!bool(m_events[event_to_use]));
+        assert(bool(m_events[event_to_use]));
         m_next_event += 1;
         return m_events[event_to_use];
     }

include/ghex/device/cuda/future.hpp

@@ -10,7 +10,7 @@
 #pragma once
 
 #include <ghex/config.hpp>
-#include <ghex/util/c_managed_struct.hpp>
+#include <ghex/device/cuda/event.hpp>
 #include <ghex/device/cuda/error.hpp>
 #ifdef GHEX_CUDACC
 #include <ghex/device/cuda/runtime.hpp>
@@ -28,16 +28,11 @@ namespace device
 template<typename T>
 struct future
 {
-    GHEX_C_MANAGED_STRUCT(
-        event_type, cudaEvent_t, [](auto&&... args)
-        { GHEX_CHECK_CUDA_RESULT(cudaEventCreateWithFlags(std::forward<decltype(args)>(args)...)) },
-        [](auto& e) { GHEX_CHECK_CUDA_RESULT_NO_THROW(cudaEventDestroy(e)) })
-
-    event_type m_event;
+    cuda_event m_event;
     T          m_data;
 
     future(T&& data, stream& stream)
-    : m_event{cudaEventDisableTiming} //: m_event{cudaEventDisableTiming | cudaEventBlockingSync}
+    : m_event{}
     , m_data{std::move(data)}
     {
         GHEX_CHECK_CUDA_RESULT(cudaEventRecord(m_event, stream));
@@ -65,16 +60,10 @@ struct future
 template<>
 struct future<void>
 {
-    GHEX_C_MANAGED_STRUCT(
-        event_type, cudaEvent_t, [](auto&&... args)
-        { GHEX_CHECK_CUDA_RESULT(cudaEventCreateWithFlags(std::forward<decltype(args)>(args)...)) },
-        [](auto& e) { GHEX_CHECK_CUDA_RESULT_NO_THROW(cudaEventDestroy(e)) })
-
-    event_type m_event;
+    cuda_event m_event;
 
     future(stream& stream)
-    : m_event{cudaEventDisableTiming}
-    //: m_event{cudaEventDisableTiming | cudaEventBlockingSync}
+    : m_event{}
     {
         GHEX_CHECK_CUDA_RESULT(cudaEventRecord(m_event, stream));
     }

include/ghex/device/cuda/stream.hpp

@@ -39,15 +39,7 @@ struct stream
         if (!m_moved) { GHEX_CHECK_CUDA_RESULT_NO_THROW(cudaStreamDestroy(m_stream)) }
     }
 
-    /**
-     * @brief	Returns `true` if `*this` has been moved, i.e. can no longer be used.
-     *
-     * @todo  The semantic of this function is a bit confusing as a valid object returns
-     *   `false`. It should be changed such that a valid object returns `true` and an
-     *   invalid one returns `false`. This is the behaviour for `GHEX_C_STRUCT` and
-     *   `GHEX_C_MANAGED_STRUCT` but not for `stream` and `cuda_event`.
-     */
-    operator bool() const noexcept { return m_moved; }
+    operator bool() const noexcept { return !m_moved; }
 
     operator cudaStream_t() const noexcept
     {