Loading [MathJax]/jax/input/TeX/config.js
cuML C++ API  23.12
All Classes Namespaces Files Functions Variables Typedefs Enumerations Enumerator Friends Macros Modules Pages
gpu.hpp
Go to the documentation of this file.
1 /*
2  * Copyright (c) 2023, 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 #pragma once
17 #include <cuda_runtime_api.h>
21 #include <stdint.h>
22 #include <type_traits>
23 
24 namespace raft_proto {
25 namespace detail {
26 
27 template <device_type dst_type, device_type src_type, typename T>
28 std::enable_if_t<
29  std::conjunction_v<std::disjunction<std::bool_constant<dst_type == device_type::gpu>,
30  std::bool_constant<src_type == device_type::gpu>>,
31  std::bool_constant<GPU_ENABLED>>,
32  void>
33 copy(T* dst, T const* src, uint32_t size, cuda_stream stream)
34 {
35  raft_proto::cuda_check(cudaMemcpyAsync(dst, src, size * sizeof(T), cudaMemcpyDefault, stream));
36 }
37 
38 } // namespace detail
39 } // namespace raft_proto
std::enable_if_t< std::conjunction_v< std::bool_constant< dst_type==device_type::cpu >, std::bool_constant< src_type==device_type::cpu > >, void > copy(T *dst, T const *src, uint32_t size, cuda_stream stream)
Definition: cpu.hpp:31
Definition: buffer.hpp:33
int cuda_stream
Definition: cuda_stream.hpp:25
void cuda_check(error_t const &err) noexcept(!GPU_ENABLED)
Definition: cuda_check.hpp:26