error.hpp

Go to the documentation of this file.

/*
 * Copyright (c) 2020-2023, NVIDIA CORPORATION.
 *
 * Licensed under the Apache License, Version 2.0 (the "License");
 * you may not use this file except in compliance with the License.
 * You may obtain a copy of the License at
 *
 *     http://www.apache.org/licenses/LICENSE-2.0
 *
 * Unless required by applicable law or agreed to in writing, software
 * distributed under the License is distributed on an "AS IS" BASIS,
 * WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
 * See the License for the specific language governing permissions and
 * limitations under the License.
 */
 
#pragma once
 
#include <cuspatial/assert.cuh>
 
#include <cuda_runtime_api.h>
 
#include <stdexcept>
#include <string>
 
namespace cuspatial {
 
struct logic_error : public std::logic_error {
  logic_error(char const* const message) : std::logic_error(message) {}
  logic_error(std::string const& message) : std::logic_error(message) {}
};
 
struct cuda_error : public std::runtime_error {
  cuda_error(std::string const& message) : std::runtime_error(message) {}
};
 
}  // namespace cuspatial
 
#define CUSPATIAL_STRINGIFY_DETAIL(x) #x
#define CUSPATIAL_STRINGIFY(x)        CUSPATIAL_STRINGIFY_DETAIL(x)
 
#define CUSPATIAL_EXPECTS(cond, reason)                                       \
  (!!(cond)) ? static_cast<void>(0)                                           \
             : throw cuspatial::logic_error("cuSpatial failure at: " __FILE__ \
                                            ":" CUSPATIAL_STRINGIFY(__LINE__) ": " reason)
 
#ifndef __CUDA_ARCH__
#define CUSPATIAL_HOST_DEVICE_EXPECTS(cond, reason) CUSPATIAL_EXPECTS(cond, reason)
#else
#define CUSPATIAL_HOST_DEVICE_EXPECTS(cond, reason) cuspatial_assert(cond&& reason)
#endif
 
#define CUSPATIAL_FAIL(reason)                                   \
  throw cuspatial::logic_error("cuSpatial failure at: " __FILE__ \
                               ":" CUSPATIAL_STRINGIFY(__LINE__) ": " reason)
 
namespace cuspatial {
namespace detail {
 
inline void throw_cuda_error(cudaError_t error, const char* file, unsigned int line)
{
  throw cuspatial::cuda_error(std::string{
    "CUDA error encountered at: " + std::string{file} + ":" + std::to_string(line) + ": " +
    std::to_string(error) + " " + cudaGetErrorName(error) + " " + cudaGetErrorString(error)});
}
 
}  // namespace detail
}  // namespace cuspatial
 
#define CUSPATIAL_CUDA_TRY(call)                                       \
  do {                                                                 \
    cudaError_t const status = (call);                                 \
    if (cudaSuccess != status) {                                       \
      cudaGetLastError();                                              \
      cuspatial::detail::throw_cuda_error(status, __FILE__, __LINE__); \
    }                                                                  \
  } while (0);
 
#ifndef NDEBUG
#define CUSPATIAL_CHECK_CUDA(stream)                   \
  do {                                                 \
    CUSPATIAL_CUDA_TRY(cudaStreamSynchronize(stream)); \
    CUSPATIAL_CUDA_TRY(cudaPeekAtLastError());         \
  } while (0);
#else
#define CUSPATIAL_CHECK_CUDA(stream) CUSPATIAL_CUDA_TRY(cudaPeekAtLastError());
#endif