19 #include <cudf/utilities/export.hpp>
22 #include <cuda_runtime_api.h>
26 #include <type_traits>
28 namespace CUDF_EXPORT
cudf {
76 explicit cuda_error(std::string
const& message, cudaError_t
const& error)
77 : std::runtime_error(message), _cudaError(error)
86 [[nodiscard]] cudaError_t
error_code()
const {
return _cudaError; }
93 using cuda_error::cuda_error;
109 explicit data_type_error(
char const*
const message) : std::invalid_argument(message) {}
116 explicit data_type_error(std::string
const& message) : std::invalid_argument(message) {}
122 #define STRINGIFY_DETAIL(x) #x
123 #define CUDF_STRINGIFY(x) STRINGIFY_DETAIL(x)
154 #define CUDF_EXPECTS(...) \
155 GET_CUDF_EXPECTS_MACRO(__VA_ARGS__, CUDF_EXPECTS_3, CUDF_EXPECTS_2) \
160 #define GET_CUDF_EXPECTS_MACRO(_1, _2, _3, NAME, ...) NAME
162 #define CUDF_EXPECTS_3(_condition, _reason, _exception_type) \
164 static_assert(std::is_base_of_v<std::exception, _exception_type>); \
165 (_condition) ? static_cast<void>(0) \
166 : throw _exception_type \
167 {"CUDF failure at: " __FILE__ ":" CUDF_STRINGIFY(__LINE__) ": " _reason}; \
170 #define CUDF_EXPECTS_2(_condition, _reason) CUDF_EXPECTS_3(_condition, _reason, cudf::logic_error)
193 #define CUDF_FAIL(...) \
194 GET_CUDF_FAIL_MACRO(__VA_ARGS__, CUDF_FAIL_2, CUDF_FAIL_1) \
199 #define GET_CUDF_FAIL_MACRO(_1, _2, NAME, ...) NAME
201 #define CUDF_FAIL_2(_what, _exception_type) \
203 throw _exception_type { "CUDF failure at:" __FILE__ ":" CUDF_STRINGIFY(__LINE__) ": " _what }
205 #define CUDF_FAIL_1(_what) CUDF_FAIL_2(_what, cudf::logic_error)
209 namespace CUDF_EXPORT
cudf {
212 inline void throw_cuda_error(cudaError_t error,
char const* file,
unsigned int line)
217 auto const last = cudaFree(
nullptr);
218 auto const msg = std::string{
"CUDA error encountered at: " + std::string{file} +
":" +
219 std::to_string(line) +
": " + std::to_string(error) +
" " +
220 cudaGetErrorName(error) +
" " + cudaGetErrorString(error)};
223 if (error == last && last == cudaDeviceSynchronize()) {
224 throw fatal_cuda_error{
"Fatal " + msg, error};
226 throw cuda_error{msg, error};
240 #define CUDF_CUDA_TRY(call) \
242 cudaError_t const status = (call); \
243 if (cudaSuccess != status) { cudf::detail::throw_cuda_error(status, __FILE__, __LINE__); } \
260 #define CUDF_CHECK_CUDA(stream) \
262 CUDF_CUDA_TRY(cudaStreamSynchronize(stream)); \
263 CUDF_CUDA_TRY(cudaPeekAtLastError()); \
266 #define CUDF_CHECK_CUDA(stream) CUDF_CUDA_TRY(cudaPeekAtLastError());
Exception thrown when a CUDA error is encountered.
cuda_error(std::string const &message, cudaError_t const &error)
Construct a new cuda error object with error message and code.
cudaError_t _cudaError
CUDA error code.
cudaError_t error_code() const
Returns the CUDA error code associated with the exception.
Exception thrown when an operation is attempted on an unsupported dtype.
data_type_error(std::string const &message)
Construct a new data_type_error object with error message.
data_type_error(char const *const message)
Constructs a data_type_error with the error message.
Exception thrown when logical precondition is violated.
logic_error(char const *const message)
Constructs a logic_error with the error message.
logic_error(std::string const &message)
Construct a new logic error object with error message.