This repository has been archived by the owner on Nov 12, 2020. It is now read-only.
-
Notifications
You must be signed in to change notification settings - Fork 6
/
preload_cudart.cpp
48 lines (41 loc) · 1.51 KB
/
preload_cudart.cpp
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
#include <cassert>
#include <cstdio>
#include <cuda_runtime.h>
#include <dlfcn.h>
#include "allocations.hpp"
#include "callbacks.hpp"
#include "driver_state.hpp"
#include "preload.hpp"
#include "thread.hpp"
#include "values.hpp"
typedef cudaError_t (*cudaFreeHostFunc)(void *ptr);
extern "C" cudaError_t cudaFreeHost(void *ptr) {
SAME_LD_PRELOAD_BOILERPLATE(cudaFreeHost);
return real_cudaFreeHost(ptr);
}
typedef cudaError_t (*cudaGetDeviceCountFunc)(int *);
extern "C" cudaError_t cudaGetDeviceCount(int *count) {
SAME_LD_PRELOAD_BOILERPLATE(cudaGetDeviceCount);
return real_cudaGetDeviceCount(count);
}
typedef cudaError_t (*cudaMallocFunc)(void **, size_t);
extern "C" cudaError_t cudaMalloc(void **devPtr, size_t size) {
SAME_LD_PRELOAD_BOILERPLATE(cudaMalloc);
return real_cudaMalloc(devPtr, size);
}
typedef cudaError_t (*cudaMallocHostFunc)(void **ptr, size_t);
extern "C" cudaError_t cudaMallocHost(void **ptr, size_t size) {
SAME_LD_PRELOAD_BOILERPLATE(cudaMallocHost);
return real_cudaMallocHost(ptr, size);
}
typedef cudaError_t (*cudaMallocManagedFunc)(void **, size_t, unsigned int);
extern "C" cudaError_t cudaMallocManaged(void **devPtr, size_t size,
unsigned int flags) {
SAME_LD_PRELOAD_BOILERPLATE(cudaMallocManaged);
return real_cudaMallocManaged(devPtr, size, flags);
}
typedef cudaError_t (*cudaSetDeviceFunc)(int device);
extern "C" cudaError_t cudaSetDevice(int device) {
SAME_LD_PRELOAD_BOILERPLATE(cudaSetDevice);
return real_cudaSetDevice(device);
}