cudadefines.hpp
2.38 KB
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
/* * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * *
* Copyright 2016 Colin Heinzmann *
* *
* 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. *
* * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * * */
#include <iostream>
using namespace std;
#include <pthread.h>
#define CUDA_SAFE_FREE(cudaPtr, errPtr) \
/*cout << pthread_self() << ": CUDA Free: " << cudaPtr << endl;*/ \
*errPtr = cudaFree(cudaPtr); \
if (*errPtr != cudaSuccess) { \
cout << pthread_self() << ": CUDA Free Error(" << *errPtr << "): " << cudaGetErrorString(*errPtr) << endl; \
throw 0; \
}
#define CUDA_SAFE_MALLOC(cudaPtrPtr, size, errPtr) \
*errPtr = cudaMalloc(cudaPtrPtr, size); \
if (*errPtr != cudaSuccess) { \
cout << pthread_self() << ": CUDA Malloc Error(" << *errPtr << "): " << cudaGetErrorString(*errPtr) << endl; \
throw 0; \
} \
//cout << pthread_self() << ": CUDA Malloc: " << (void*)*(int**)cudaPtrPtr << endl;
#define CUDA_SAFE_MEMCPY(dstPtr, srcPtr, count, kind, errPtr) \
*errPtr = cudaMemcpy(dstPtr, srcPtr, count, kind); \
if (*errPtr != cudaSuccess) { \
cout << pthread_self() << ": CUDA Memcpy Error(" << *errPtr << "): " << cudaGetErrorString(*errPtr) << endl; \
throw 0; \
}
#define CUDA_KERNEL_ERR_CHK(errPtr) \
*errPtr = cudaPeekAtLastError(); \
if (*errPtr != cudaSuccess) { \
cout << pthread_self() << ": Kernel Call Err(" << *errPtr << "): " << cudaGetErrorString(*errPtr) << endl; \
throw 0; \
}