cuda_stream.hpp
Go to the documentation of this file.
1 /*
2  * Copyright (c) 2020-2025, NVIDIA CORPORATION.
3  *
4  * Licensed under the Apache License, Version 2.0 (the "License");
5  * you may not use this file except in compliance with the License.
6  * You may obtain a copy of the License at
7  *
8  * http://www.apache.org/licenses/LICENSE-2.0
9  *
10  * Unless required by applicable law or agreed to in writing, software
11  * distributed under the License is distributed on an "AS IS" BASIS,
12  * WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
13  * See the License for the specific language governing permissions and
14  * limitations under the License.
15  */
16 
17 #pragma once
18 
19 #include <rmm/cuda_stream_view.hpp>
20 #include <rmm/detail/export.hpp>
21 
22 #include <cuda_runtime_api.h>
23 
24 #include <functional>
25 #include <memory>
26 
27 namespace RMM_EXPORT rmm {
39 class cuda_stream {
40  public:
47  cuda_stream(cuda_stream&&) = default;
57  ~cuda_stream() = default;
58  cuda_stream(cuda_stream const&) = delete; // Copying disallowed: one stream one owner
59  cuda_stream& operator=(cuda_stream&) = delete;
60 
67 
74  [[nodiscard]] bool is_valid() const;
75 
81  [[nodiscard]] cudaStream_t value() const;
82 
86  explicit operator cudaStream_t() const noexcept;
87 
93  [[nodiscard]] cuda_stream_view view() const;
94 
100  operator cuda_stream_view() const;
101 
109  void synchronize() const;
110 
116  void synchronize_no_throw() const noexcept;
117 
118  private:
119  std::unique_ptr<cudaStream_t, std::function<void(cudaStream_t*)>> stream_;
120 };
121  // end of group
123 } // namespace RMM_EXPORT rmm
Strongly-typed non-owning wrapper for CUDA streams with default constructor.
Definition: cuda_stream_view.hpp:39
Owning wrapper for a CUDA stream.
Definition: cuda_stream.hpp:39
bool is_valid() const
Returns true if the owned stream is non-null.
cuda_stream()
Construct a new cuda stream object.
cuda_stream & operator=(cuda_stream &&)=default
Move copy assignment operator (default)
cudaStream_t value() const
Get the value of the wrapped CUDA stream.
cuda_stream(cuda_stream &&)=default
Move constructor (default)