| #pragma once |
|
|
| #include <stdio.h> |
|
|
| #if defined(__HIPCC__) |
| #define HOST_DEVICE_INLINE __host__ __device__ |
| #define DEVICE_INLINE __device__ |
| #define HOST_INLINE __host__ |
| #elif defined(__CUDACC__) || defined(_NVHPC_CUDA) |
| #define HOST_DEVICE_INLINE __host__ __device__ __forceinline__ |
| #define DEVICE_INLINE __device__ __forceinline__ |
| #define HOST_INLINE __host__ __forceinline__ |
| #else |
| #define HOST_DEVICE_INLINE inline |
| #define DEVICE_INLINE inline |
| #define HOST_INLINE inline |
| #endif |
|
|
| #define CUDA_CHECK(cmd) \ |
| do { \ |
| cudaError_t e = cmd; \ |
| if (e != cudaSuccess) { \ |
| printf("Failed: Cuda error %s:%d '%s'\n", __FILE__, __LINE__, \ |
| cudaGetErrorString(e)); \ |
| exit(EXIT_FAILURE); \ |
| } \ |
| } while (0) |
|
|
| int64_t get_device_attribute(int64_t attribute, int64_t device_id); |
|
|
| int64_t get_max_shared_memory_per_block_device_attribute(int64_t device_id); |
|
|
| namespace cuda_utils { |
|
|
| template <typename T> |
| HOST_DEVICE_INLINE constexpr std::enable_if_t<std::is_integral_v<T>, T> |
| ceil_div(T a, T b) { |
| return (a + b - 1) / b; |
| } |
|
|
| }; |
