/*
 *  Copyright 2008-2013 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 <thrust/detail/config.h>

#if defined(_CCCL_IMPLICIT_SYSTEM_HEADER_GCC)
#  pragma GCC system_header
#elif defined(_CCCL_IMPLICIT_SYSTEM_HEADER_CLANG)
#  pragma clang system_header
#elif defined(_CCCL_IMPLICIT_SYSTEM_HEADER_MSVC)
#  pragma system_header
#endif // no system header

#include <thrust/system/cuda/error.h>

THRUST_NAMESPACE_BEGIN

namespace system
{

error_code make_error_code(cuda::errc::errc_t e)
{
  return error_code(static_cast<int>(e), cuda_category());
} // end make_error_code()

error_condition make_error_condition(cuda::errc::errc_t e)
{
  return error_condition(static_cast<int>(e), cuda_category());
} // end make_error_condition()

namespace cuda_cub
{

namespace detail
{

class cuda_error_category : public error_category
{
public:
  inline cuda_error_category() {}

  inline virtual const char* name() const
  {
    return "cuda";
  }

  inline virtual std::string message(int ev) const
  {
    char const* const unknown_str  = "unknown error";
    char const* const unknown_name = "cudaErrorUnknown";
    char const* c_str              = ::cudaGetErrorString(static_cast<cudaError_t>(ev));
    char const* c_name             = ::cudaGetErrorName(static_cast<cudaError_t>(ev));
    return std::string(c_name ? c_name : unknown_name) + ": " + (c_str ? c_str : unknown_str);
  }

  inline virtual error_condition default_error_condition(int ev) const
  {
    using namespace cuda::errc;

    if (ev < ::cudaErrorUnknown)
    {
      return make_error_condition(static_cast<errc_t>(ev));
    }

    return system_category().default_error_condition(ev);
  }
}; // end cuda_error_category

} // namespace detail

} // end namespace cuda_cub

const error_category& cuda_category()
{
  static const thrust::system::cuda_cub::detail::cuda_error_category result;
  return result;
}

} // end namespace system

THRUST_NAMESPACE_END