CUB
 All Classes Namespaces Files Functions Variables Typedefs Enumerations Enumerator Friends Groups
util_debug.cuh
Go to the documentation of this file.
1 /******************************************************************************
2  * Copyright (c) 2011, Duane Merrill. All rights reserved.
3  * Copyright (c) 2011-2015, NVIDIA CORPORATION. All rights reserved.
4  *
5  * Redistribution and use in source and binary forms, with or without
6  * modification, are permitted provided that the following conditions are met:
7  * * Redistributions of source code must retain the above copyright
8  * notice, this list of conditions and the following disclaimer.
9  * * Redistributions in binary form must reproduce the above copyright
10  * notice, this list of conditions and the following disclaimer in the
11  * documentation and/or other materials provided with the distribution.
12  * * Neither the name of the NVIDIA CORPORATION nor the
13  * names of its contributors may be used to endorse or promote products
14  * derived from this software without specific prior written permission.
15  *
16  * THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS "AS IS" AND
17  * ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT LIMITED TO, THE IMPLIED
18  * WARRANTIES OF MERCHANTABILITY AND FITNESS FOR A PARTICULAR PURPOSE ARE
19  * DISCLAIMED. IN NO EVENT SHALL NVIDIA CORPORATION BE LIABLE FOR ANY
20  * DIRECT, INDIRECT, INCIDENTAL, SPECIAL, EXEMPLARY, OR CONSEQUENTIAL DAMAGES
21  * (INCLUDING, BUT NOT LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES;
22  * LOSS OF USE, DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND
23  * ON ANY THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT
24  * (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS
25  * SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
26  *
27  ******************************************************************************/
28 
37 #pragma once
38 
39 #include <stdio.h>
40 #include "util_namespace.cuh"
41 #include "util_arch.cuh"
42 
44 CUB_NS_PREFIX
45 
47 namespace cub {
48 
49 
56 #if (defined(DEBUG) || defined(_DEBUG)) && !defined(CUB_STDERR)
58  #define CUB_STDERR
59 #endif
60 
61 
62 
68 __host__ __device__ __forceinline__ cudaError_t Debug(
69  cudaError_t error,
70  const char* filename,
71  int line)
72 {
73 #ifdef CUB_STDERR
74  if (error)
75  {
76  #if (CUB_PTX_ARCH == 0)
77  fprintf(stderr, "CUDA error %d [%s, %d]: %s\n", error, filename, line, cudaGetErrorString(error));
78  fflush(stderr);
79  #elif (CUB_PTX_ARCH >= 200)
80  printf("CUDA error %d [block (%d,%d,%d) thread (%d,%d,%d), %s, %d]\n", error, blockIdx.z, blockIdx.y, blockIdx.x, threadIdx.z, threadIdx.y, threadIdx.x, filename, line);
81  #endif
82  }
83 #endif
84  return error;
85 }
86 
87 
91 #ifndef CubDebug
92  #define CubDebug(e) cub::Debug((e), __FILE__, __LINE__)
93 #endif
94 
95 
99 #ifndef CubDebugExit
100  #define CubDebugExit(e) if (cub::Debug((e), __FILE__, __LINE__)) { exit(1); }
101 #endif
102 
103 
107 #if !defined(_CubLog)
108  #if (CUB_PTX_ARCH == 0)
109  #define _CubLog(format, ...) printf(format,__VA_ARGS__);
110  #elif (CUB_PTX_ARCH >= 200)
111  #define _CubLog(format, ...) printf("[block (%d,%d,%d), thread (%d,%d,%d)]: " format, blockIdx.z, blockIdx.y, blockIdx.x, threadIdx.z, threadIdx.y, threadIdx.x, __VA_ARGS__);
112  #endif
113 #endif
114 
115 
116 
117  // end group UtilMgmt
119 
120 } // CUB namespace
121 CUB_NS_POSTFIX // Optional outer namespace(s)