2 #ifndef _HIP_PROF_STR_H 3 #define _HIP_PROF_STR_H 6 #define INIT_NONE_CB_ARGS_DATA(cb_data) {}; 7 #define INIT_hipModuleGetFunctionEx_CB_ARGS_DATA(cb_data) {}; 8 #define INIT_hipDestroyTextureObject_CB_ARGS_DATA(cb_data) {}; 9 #define INIT_hipTexRefSetAddress_CB_ARGS_DATA(cb_data) {}; 10 #define INIT_hipBindTexture2D_CB_ARGS_DATA(cb_data) {}; 11 #define INIT_hipTexRefGetArray_CB_ARGS_DATA(cb_data) {}; 12 #define INIT_hipCreateTextureObject_CB_ARGS_DATA(cb_data) {}; 13 #define INIT_hipBindTextureToMipmappedArray_CB_ARGS_DATA(cb_data) {}; 14 #define INIT_hipBindTextureToArray_CB_ARGS_DATA(cb_data) {}; 15 #define INIT_hipTexRefSetFormat_CB_ARGS_DATA(cb_data) {}; 16 #define INIT_hipMemcpyHtoH_CB_ARGS_DATA(cb_data) {}; 17 #define INIT_hipGetTextureReference_CB_ARGS_DATA(cb_data) {}; 18 #define INIT_hipTexRefSetArray_CB_ARGS_DATA(cb_data) {}; 19 #define INIT_hipHccGetAcceleratorView_CB_ARGS_DATA(cb_data) {}; 20 #define INIT_hipTexRefSetAddress2D_CB_ARGS_DATA(cb_data) {}; 21 #define INIT_hipGetTextureObjectResourceViewDesc_CB_ARGS_DATA(cb_data) {}; 22 #define INIT_hipUnbindTexture_CB_ARGS_DATA(cb_data) {}; 23 #define INIT_hipTexRefSetFilterMode_CB_ARGS_DATA(cb_data) {}; 24 #define INIT_hipGetTextureAlignmentOffset_CB_ARGS_DATA(cb_data) {}; 25 #define INIT_hipCreateSurfaceObject_CB_ARGS_DATA(cb_data) {}; 26 #define INIT_hipGetChannelDesc_CB_ARGS_DATA(cb_data) {}; 27 #define INIT_hipTexRefGetAddressMode_CB_ARGS_DATA(cb_data) {}; 28 #define INIT_hipGetTextureObjectResourceDesc_CB_ARGS_DATA(cb_data) {}; 29 #define INIT_hipDestroySurfaceObject_CB_ARGS_DATA(cb_data) {}; 30 #define INIT_hipTexRefSetAddressMode_CB_ARGS_DATA(cb_data) {}; 31 #define INIT_hipTexRefSetFlags_CB_ARGS_DATA(cb_data) {}; 32 #define INIT_hipBindTexture_CB_ARGS_DATA(cb_data) {}; 33 #define INIT_hipHccGetAccelerator_CB_ARGS_DATA(cb_data) {}; 34 #define INIT_hipTexRefGetAddress_CB_ARGS_DATA(cb_data) {}; 35 #define INIT_hipGetTextureObjectTextureDesc_CB_ARGS_DATA(cb_data) {}; 39 HIP_API_ID_hipStreamCreateWithPriority = 0,
40 HIP_API_ID_hipMemcpyToSymbolAsync = 1,
41 HIP_API_ID_hipMallocPitch = 2,
42 HIP_API_ID_hipMalloc = 3,
43 HIP_API_ID_hipMemsetD16 = 4,
44 HIP_API_ID_hipDeviceGetName = 5,
45 HIP_API_ID_hipEventRecord = 6,
46 HIP_API_ID_hipCtxSynchronize = 7,
47 HIP_API_ID_hipDrvOccupancyMaxActiveBlocksPerMultiprocessor = 8,
48 HIP_API_ID_hipSetDevice = 9,
49 HIP_API_ID_hipCtxGetApiVersion = 10,
50 HIP_API_ID_hipSetupArgument = 11,
51 HIP_API_ID_hipMemcpyFromSymbolAsync = 12,
52 HIP_API_ID_hipExtGetLinkTypeAndHopCount = 13,
53 HIP_API_ID_hipMemcpyDtoD = 14,
54 HIP_API_ID_hipHostFree = 15,
55 HIP_API_ID_hipMemcpy2DToArray = 16,
56 HIP_API_ID_hipMemsetD8Async = 17,
57 HIP_API_ID_hipCtxGetCacheConfig = 18,
58 HIP_API_ID_hipStreamWaitEvent = 19,
59 HIP_API_ID_hipDeviceGetStreamPriorityRange = 20,
60 HIP_API_ID_hipModuleLoad = 21,
61 HIP_API_ID_hipDevicePrimaryCtxSetFlags = 22,
62 HIP_API_ID_hipLaunchCooperativeKernel = 23,
63 HIP_API_ID_hipLaunchCooperativeKernelMultiDevice = 24,
64 HIP_API_ID_hipMemcpyAsync = 25,
65 HIP_API_ID_hipMalloc3DArray = 26,
66 HIP_API_ID_hipStreamCreate = 27,
67 HIP_API_ID_hipCtxGetCurrent = 28,
68 HIP_API_ID_hipDevicePrimaryCtxGetState = 29,
69 HIP_API_ID_hipEventQuery = 30,
70 HIP_API_ID_hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags = 31,
71 HIP_API_ID_hipEventCreate = 32,
72 HIP_API_ID_hipMemGetAddressRange = 33,
73 HIP_API_ID_hipMemcpyFromSymbol = 34,
74 HIP_API_ID_hipArrayCreate = 35,
75 HIP_API_ID_hipStreamGetFlags = 36,
76 HIP_API_ID_hipMallocArray = 37,
77 HIP_API_ID_hipCtxGetSharedMemConfig = 38,
78 HIP_API_ID_hipMemPtrGetInfo = 39,
79 HIP_API_ID_hipFuncGetAttribute = 40,
80 HIP_API_ID_hipCtxGetFlags = 41,
81 HIP_API_ID_hipStreamDestroy = 42,
82 HIP_API_ID___hipPushCallConfiguration = 43,
83 HIP_API_ID_hipMemset3DAsync = 44,
84 HIP_API_ID_hipMemcpy3D = 45,
85 HIP_API_ID_hipInit = 46,
86 HIP_API_ID_hipMemcpyAtoH = 47,
87 HIP_API_ID_hipStreamGetPriority = 48,
88 HIP_API_ID_hipMemset2D = 49,
89 HIP_API_ID_hipMemset2DAsync = 50,
90 HIP_API_ID_hipDeviceCanAccessPeer = 51,
91 HIP_API_ID_hipDeviceEnablePeerAccess = 52,
92 HIP_API_ID_hipLaunchKernel = 53,
93 HIP_API_ID_hipMemsetD16Async = 54,
94 HIP_API_ID_hipModuleUnload = 55,
95 HIP_API_ID_hipHostUnregister = 56,
96 HIP_API_ID_hipProfilerStop = 57,
97 HIP_API_ID_hipLaunchByPtr = 58,
98 HIP_API_ID_hipStreamSynchronize = 59,
99 HIP_API_ID_hipDeviceSetCacheConfig = 60,
100 HIP_API_ID_hipGetErrorName = 61,
101 HIP_API_ID_hipMemcpyHtoD = 62,
102 HIP_API_ID_hipModuleGetGlobal = 63,
103 HIP_API_ID_hipMemcpyHtoA = 64,
104 HIP_API_ID_hipCtxCreate = 65,
105 HIP_API_ID_hipMemcpy2D = 66,
106 HIP_API_ID_hipIpcCloseMemHandle = 67,
107 HIP_API_ID_hipChooseDevice = 68,
108 HIP_API_ID_hipGetLastError = 69,
109 HIP_API_ID_hipDeviceComputeCapability = 70,
110 HIP_API_ID_hipDeviceGet = 71,
111 HIP_API_ID_hipProfilerStart = 72,
112 HIP_API_ID_hipCtxSetCacheConfig = 73,
113 HIP_API_ID_hipFuncSetCacheConfig = 74,
114 HIP_API_ID_hipModuleGetTexRef = 75,
115 HIP_API_ID_hipMemcpyPeerAsync = 76,
116 HIP_API_ID_hipMemcpyWithStream = 77,
117 HIP_API_ID_hipDevicePrimaryCtxReset = 78,
118 HIP_API_ID_hipMemcpy3DAsync = 79,
119 HIP_API_ID_hipEventDestroy = 80,
120 HIP_API_ID_hipCtxPopCurrent = 81,
121 HIP_API_ID_hipGetSymbolAddress = 82,
122 HIP_API_ID_hipHostGetFlags = 83,
123 HIP_API_ID_hipHostMalloc = 84,
124 HIP_API_ID_hipDriverGetVersion = 85,
125 HIP_API_ID_hipMemGetInfo = 86,
126 HIP_API_ID_hipDeviceReset = 87,
127 HIP_API_ID_hipMemset = 88,
128 HIP_API_ID_hipMemsetD8 = 89,
129 HIP_API_ID_hipMemcpyParam2DAsync = 90,
130 HIP_API_ID_hipHostRegister = 91,
131 HIP_API_ID_hipCtxSetSharedMemConfig = 92,
132 HIP_API_ID_hipArray3DCreate = 93,
133 HIP_API_ID_hipIpcOpenMemHandle = 94,
134 HIP_API_ID_hipDeviceSetSharedMemConfig = 95,
135 HIP_API_ID_hipCtxDestroy = 96,
136 HIP_API_ID_hipDeviceGetSharedMemConfig = 97,
137 HIP_API_ID_hipMemcpy2DFromArray = 98,
138 HIP_API_ID_hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags = 99,
139 HIP_API_ID_hipSetDeviceFlags = 100,
140 HIP_API_ID_hipHccModuleLaunchKernel = 101,
141 HIP_API_ID_hipFree = 102,
142 HIP_API_ID_hipOccupancyMaxPotentialBlockSize = 103,
143 HIP_API_ID_hipDeviceGetAttribute = 104,
144 HIP_API_ID_hipMemcpyDtoH = 105,
145 HIP_API_ID_hipCtxDisablePeerAccess = 106,
146 HIP_API_ID_hipMallocManaged = 107,
147 HIP_API_ID_hipDeviceGetByPCIBusId = 108,
148 HIP_API_ID_hipIpcGetMemHandle = 109,
149 HIP_API_ID_hipMemcpyHtoDAsync = 110,
150 HIP_API_ID_hipCtxGetDevice = 111,
151 HIP_API_ID_hipMemset3D = 112,
152 HIP_API_ID_hipModuleLoadData = 113,
153 HIP_API_ID_hipDeviceTotalMem = 114,
154 HIP_API_ID_hipOccupancyMaxActiveBlocksPerMultiprocessor = 115,
155 HIP_API_ID_hipCtxSetCurrent = 116,
156 HIP_API_ID_hipGetErrorString = 117,
157 HIP_API_ID_hipDevicePrimaryCtxRetain = 118,
158 HIP_API_ID_hipDeviceDisablePeerAccess = 119,
159 HIP_API_ID_hipStreamCreateWithFlags = 120,
160 HIP_API_ID_hipMemcpyFromArray = 121,
161 HIP_API_ID_hipMemcpy2DAsync = 122,
162 HIP_API_ID_hipFuncGetAttributes = 123,
163 HIP_API_ID_hipGetSymbolSize = 124,
164 HIP_API_ID_hipEventCreateWithFlags = 125,
165 HIP_API_ID_hipStreamQuery = 126,
166 HIP_API_ID_hipDeviceGetPCIBusId = 127,
167 HIP_API_ID_hipMemcpy = 128,
168 HIP_API_ID_hipPeekAtLastError = 129,
169 HIP_API_ID_hipExtLaunchMultiKernelMultiDevice = 130,
170 HIP_API_ID_hipStreamAddCallback = 131,
171 HIP_API_ID_hipMemcpyToArray = 132,
172 HIP_API_ID_hipMemsetD32 = 133,
173 HIP_API_ID_hipExtModuleLaunchKernel = 134,
174 HIP_API_ID_hipDeviceSynchronize = 135,
175 HIP_API_ID_hipDeviceGetCacheConfig = 136,
176 HIP_API_ID_hipMalloc3D = 137,
177 HIP_API_ID_hipPointerGetAttributes = 138,
178 HIP_API_ID_hipMemsetAsync = 139,
179 HIP_API_ID_hipMemcpyToSymbol = 140,
180 HIP_API_ID_hipCtxPushCurrent = 141,
181 HIP_API_ID_hipMemcpyPeer = 142,
182 HIP_API_ID_hipEventSynchronize = 143,
183 HIP_API_ID_hipMemcpyDtoDAsync = 144,
184 HIP_API_ID_hipExtMallocWithFlags = 145,
185 HIP_API_ID_hipCtxEnablePeerAccess = 146,
186 HIP_API_ID_hipMemcpyDtoHAsync = 147,
187 HIP_API_ID_hipModuleLaunchKernel = 148,
188 HIP_API_ID_hipMemAllocPitch = 149,
189 HIP_API_ID_hipMemcpy2DFromArrayAsync = 150,
190 HIP_API_ID_hipDeviceGetLimit = 151,
191 HIP_API_ID_hipModuleLoadDataEx = 152,
192 HIP_API_ID_hipRuntimeGetVersion = 153,
193 HIP_API_ID___hipPopCallConfiguration = 154,
194 HIP_API_ID_hipGetDeviceProperties = 155,
195 HIP_API_ID_hipFreeArray = 156,
196 HIP_API_ID_hipEventElapsedTime = 157,
197 HIP_API_ID_hipDevicePrimaryCtxRelease = 158,
198 HIP_API_ID_hipHostGetDevicePointer = 159,
199 HIP_API_ID_hipMemcpyParam2D = 160,
200 HIP_API_ID_hipModuleGetFunction = 161,
201 HIP_API_ID_hipMemsetD32Async = 162,
202 HIP_API_ID_hipGetDevice = 163,
203 HIP_API_ID_hipGetDeviceCount = 164,
204 HIP_API_ID_NUMBER = 165,
206 HIP_API_ID_NONE = HIP_API_ID_NUMBER,
207 HIP_API_ID_hipModuleGetFunctionEx = HIP_API_ID_NUMBER,
208 HIP_API_ID_hipDestroyTextureObject = HIP_API_ID_NUMBER,
209 HIP_API_ID_hipTexRefSetAddress = HIP_API_ID_NUMBER,
210 HIP_API_ID_hipBindTexture2D = HIP_API_ID_NUMBER,
211 HIP_API_ID_hipTexRefGetArray = HIP_API_ID_NUMBER,
212 HIP_API_ID_hipCreateTextureObject = HIP_API_ID_NUMBER,
213 HIP_API_ID_hipBindTextureToMipmappedArray = HIP_API_ID_NUMBER,
214 HIP_API_ID_hipBindTextureToArray = HIP_API_ID_NUMBER,
215 HIP_API_ID_hipTexRefSetFormat = HIP_API_ID_NUMBER,
216 HIP_API_ID_hipMemcpyHtoH = HIP_API_ID_NUMBER,
217 HIP_API_ID_hipGetTextureReference = HIP_API_ID_NUMBER,
218 HIP_API_ID_hipTexRefSetArray = HIP_API_ID_NUMBER,
219 HIP_API_ID_hipHccGetAcceleratorView = HIP_API_ID_NUMBER,
220 HIP_API_ID_hipTexRefSetAddress2D = HIP_API_ID_NUMBER,
221 HIP_API_ID_hipGetTextureObjectResourceViewDesc = HIP_API_ID_NUMBER,
222 HIP_API_ID_hipUnbindTexture = HIP_API_ID_NUMBER,
223 HIP_API_ID_hipTexRefSetFilterMode = HIP_API_ID_NUMBER,
224 HIP_API_ID_hipGetTextureAlignmentOffset = HIP_API_ID_NUMBER,
225 HIP_API_ID_hipCreateSurfaceObject = HIP_API_ID_NUMBER,
226 HIP_API_ID_hipGetChannelDesc = HIP_API_ID_NUMBER,
227 HIP_API_ID_hipTexRefGetAddressMode = HIP_API_ID_NUMBER,
228 HIP_API_ID_hipGetTextureObjectResourceDesc = HIP_API_ID_NUMBER,
229 HIP_API_ID_hipDestroySurfaceObject = HIP_API_ID_NUMBER,
230 HIP_API_ID_hipTexRefSetAddressMode = HIP_API_ID_NUMBER,
231 HIP_API_ID_hipTexRefSetFlags = HIP_API_ID_NUMBER,
232 HIP_API_ID_hipBindTexture = HIP_API_ID_NUMBER,
233 HIP_API_ID_hipHccGetAccelerator = HIP_API_ID_NUMBER,
234 HIP_API_ID_hipTexRefGetAddress = HIP_API_ID_NUMBER,
235 HIP_API_ID_hipGetTextureObjectTextureDesc = HIP_API_ID_NUMBER,
239 static inline const char* hip_api_name(
const uint32_t
id) {
241 case HIP_API_ID_hipStreamCreateWithPriority:
return "hipStreamCreateWithPriority";
242 case HIP_API_ID_hipMemcpyToSymbolAsync:
return "hipMemcpyToSymbolAsync";
243 case HIP_API_ID_hipMallocPitch:
return "hipMallocPitch";
244 case HIP_API_ID_hipMalloc:
return "hipMalloc";
245 case HIP_API_ID_hipMemsetD16:
return "hipMemsetD16";
246 case HIP_API_ID_hipDeviceGetName:
return "hipDeviceGetName";
247 case HIP_API_ID_hipEventRecord:
return "hipEventRecord";
248 case HIP_API_ID_hipCtxSynchronize:
return "hipCtxSynchronize";
249 case HIP_API_ID_hipDrvOccupancyMaxActiveBlocksPerMultiprocessor:
return "hipDrvOccupancyMaxActiveBlocksPerMultiprocessor";
250 case HIP_API_ID_hipSetDevice:
return "hipSetDevice";
251 case HIP_API_ID_hipCtxGetApiVersion:
return "hipCtxGetApiVersion";
252 case HIP_API_ID_hipSetupArgument:
return "hipSetupArgument";
253 case HIP_API_ID_hipMemcpyFromSymbolAsync:
return "hipMemcpyFromSymbolAsync";
254 case HIP_API_ID_hipExtGetLinkTypeAndHopCount:
return "hipExtGetLinkTypeAndHopCount";
255 case HIP_API_ID_hipMemcpyDtoD:
return "hipMemcpyDtoD";
256 case HIP_API_ID_hipHostFree:
return "hipHostFree";
257 case HIP_API_ID_hipMemcpy2DToArray:
return "hipMemcpy2DToArray";
258 case HIP_API_ID_hipMemsetD8Async:
return "hipMemsetD8Async";
259 case HIP_API_ID_hipCtxGetCacheConfig:
return "hipCtxGetCacheConfig";
260 case HIP_API_ID_hipStreamWaitEvent:
return "hipStreamWaitEvent";
261 case HIP_API_ID_hipDeviceGetStreamPriorityRange:
return "hipDeviceGetStreamPriorityRange";
262 case HIP_API_ID_hipModuleLoad:
return "hipModuleLoad";
263 case HIP_API_ID_hipDevicePrimaryCtxSetFlags:
return "hipDevicePrimaryCtxSetFlags";
264 case HIP_API_ID_hipLaunchCooperativeKernel:
return "hipLaunchCooperativeKernel";
265 case HIP_API_ID_hipLaunchCooperativeKernelMultiDevice:
return "hipLaunchCooperativeKernelMultiDevice";
266 case HIP_API_ID_hipMemcpyAsync:
return "hipMemcpyAsync";
267 case HIP_API_ID_hipMalloc3DArray:
return "hipMalloc3DArray";
268 case HIP_API_ID_hipStreamCreate:
return "hipStreamCreate";
269 case HIP_API_ID_hipCtxGetCurrent:
return "hipCtxGetCurrent";
270 case HIP_API_ID_hipDevicePrimaryCtxGetState:
return "hipDevicePrimaryCtxGetState";
271 case HIP_API_ID_hipEventQuery:
return "hipEventQuery";
272 case HIP_API_ID_hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags:
return "hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags";
273 case HIP_API_ID_hipEventCreate:
return "hipEventCreate";
274 case HIP_API_ID_hipMemGetAddressRange:
return "hipMemGetAddressRange";
275 case HIP_API_ID_hipMemcpyFromSymbol:
return "hipMemcpyFromSymbol";
276 case HIP_API_ID_hipArrayCreate:
return "hipArrayCreate";
277 case HIP_API_ID_hipStreamGetFlags:
return "hipStreamGetFlags";
278 case HIP_API_ID_hipMallocArray:
return "hipMallocArray";
279 case HIP_API_ID_hipCtxGetSharedMemConfig:
return "hipCtxGetSharedMemConfig";
280 case HIP_API_ID_hipMemPtrGetInfo:
return "hipMemPtrGetInfo";
281 case HIP_API_ID_hipFuncGetAttribute:
return "hipFuncGetAttribute";
282 case HIP_API_ID_hipCtxGetFlags:
return "hipCtxGetFlags";
283 case HIP_API_ID_hipStreamDestroy:
return "hipStreamDestroy";
284 case HIP_API_ID___hipPushCallConfiguration:
return "__hipPushCallConfiguration";
285 case HIP_API_ID_hipMemset3DAsync:
return "hipMemset3DAsync";
286 case HIP_API_ID_hipMemcpy3D:
return "hipMemcpy3D";
287 case HIP_API_ID_hipInit:
return "hipInit";
288 case HIP_API_ID_hipMemcpyAtoH:
return "hipMemcpyAtoH";
289 case HIP_API_ID_hipStreamGetPriority:
return "hipStreamGetPriority";
290 case HIP_API_ID_hipMemset2D:
return "hipMemset2D";
291 case HIP_API_ID_hipMemset2DAsync:
return "hipMemset2DAsync";
292 case HIP_API_ID_hipDeviceCanAccessPeer:
return "hipDeviceCanAccessPeer";
293 case HIP_API_ID_hipDeviceEnablePeerAccess:
return "hipDeviceEnablePeerAccess";
294 case HIP_API_ID_hipLaunchKernel:
return "hipLaunchKernel";
295 case HIP_API_ID_hipMemsetD16Async:
return "hipMemsetD16Async";
296 case HIP_API_ID_hipModuleUnload:
return "hipModuleUnload";
297 case HIP_API_ID_hipHostUnregister:
return "hipHostUnregister";
298 case HIP_API_ID_hipProfilerStop:
return "hipProfilerStop";
299 case HIP_API_ID_hipLaunchByPtr:
return "hipLaunchByPtr";
300 case HIP_API_ID_hipStreamSynchronize:
return "hipStreamSynchronize";
301 case HIP_API_ID_hipDeviceSetCacheConfig:
return "hipDeviceSetCacheConfig";
302 case HIP_API_ID_hipGetErrorName:
return "hipGetErrorName";
303 case HIP_API_ID_hipMemcpyHtoD:
return "hipMemcpyHtoD";
304 case HIP_API_ID_hipModuleGetGlobal:
return "hipModuleGetGlobal";
305 case HIP_API_ID_hipMemcpyHtoA:
return "hipMemcpyHtoA";
306 case HIP_API_ID_hipCtxCreate:
return "hipCtxCreate";
307 case HIP_API_ID_hipMemcpy2D:
return "hipMemcpy2D";
308 case HIP_API_ID_hipIpcCloseMemHandle:
return "hipIpcCloseMemHandle";
309 case HIP_API_ID_hipChooseDevice:
return "hipChooseDevice";
310 case HIP_API_ID_hipGetLastError:
return "hipGetLastError";
311 case HIP_API_ID_hipDeviceComputeCapability:
return "hipDeviceComputeCapability";
312 case HIP_API_ID_hipDeviceGet:
return "hipDeviceGet";
313 case HIP_API_ID_hipProfilerStart:
return "hipProfilerStart";
314 case HIP_API_ID_hipCtxSetCacheConfig:
return "hipCtxSetCacheConfig";
315 case HIP_API_ID_hipFuncSetCacheConfig:
return "hipFuncSetCacheConfig";
316 case HIP_API_ID_hipModuleGetTexRef:
return "hipModuleGetTexRef";
317 case HIP_API_ID_hipMemcpyPeerAsync:
return "hipMemcpyPeerAsync";
318 case HIP_API_ID_hipMemcpyWithStream:
return "hipMemcpyWithStream";
319 case HIP_API_ID_hipDevicePrimaryCtxReset:
return "hipDevicePrimaryCtxReset";
320 case HIP_API_ID_hipMemcpy3DAsync:
return "hipMemcpy3DAsync";
321 case HIP_API_ID_hipEventDestroy:
return "hipEventDestroy";
322 case HIP_API_ID_hipCtxPopCurrent:
return "hipCtxPopCurrent";
323 case HIP_API_ID_hipGetSymbolAddress:
return "hipGetSymbolAddress";
324 case HIP_API_ID_hipHostGetFlags:
return "hipHostGetFlags";
325 case HIP_API_ID_hipHostMalloc:
return "hipHostMalloc";
326 case HIP_API_ID_hipDriverGetVersion:
return "hipDriverGetVersion";
327 case HIP_API_ID_hipMemGetInfo:
return "hipMemGetInfo";
328 case HIP_API_ID_hipDeviceReset:
return "hipDeviceReset";
329 case HIP_API_ID_hipMemset:
return "hipMemset";
330 case HIP_API_ID_hipMemsetD8:
return "hipMemsetD8";
331 case HIP_API_ID_hipMemcpyParam2DAsync:
return "hipMemcpyParam2DAsync";
332 case HIP_API_ID_hipHostRegister:
return "hipHostRegister";
333 case HIP_API_ID_hipCtxSetSharedMemConfig:
return "hipCtxSetSharedMemConfig";
334 case HIP_API_ID_hipArray3DCreate:
return "hipArray3DCreate";
335 case HIP_API_ID_hipIpcOpenMemHandle:
return "hipIpcOpenMemHandle";
336 case HIP_API_ID_hipDeviceSetSharedMemConfig:
return "hipDeviceSetSharedMemConfig";
337 case HIP_API_ID_hipCtxDestroy:
return "hipCtxDestroy";
338 case HIP_API_ID_hipDeviceGetSharedMemConfig:
return "hipDeviceGetSharedMemConfig";
339 case HIP_API_ID_hipMemcpy2DFromArray:
return "hipMemcpy2DFromArray";
340 case HIP_API_ID_hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags:
return "hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags";
341 case HIP_API_ID_hipSetDeviceFlags:
return "hipSetDeviceFlags";
342 case HIP_API_ID_hipHccModuleLaunchKernel:
return "hipHccModuleLaunchKernel";
343 case HIP_API_ID_hipFree:
return "hipFree";
344 case HIP_API_ID_hipOccupancyMaxPotentialBlockSize:
return "hipOccupancyMaxPotentialBlockSize";
345 case HIP_API_ID_hipDeviceGetAttribute:
return "hipDeviceGetAttribute";
346 case HIP_API_ID_hipMemcpyDtoH:
return "hipMemcpyDtoH";
347 case HIP_API_ID_hipCtxDisablePeerAccess:
return "hipCtxDisablePeerAccess";
348 case HIP_API_ID_hipMallocManaged:
return "hipMallocManaged";
349 case HIP_API_ID_hipDeviceGetByPCIBusId:
return "hipDeviceGetByPCIBusId";
350 case HIP_API_ID_hipIpcGetMemHandle:
return "hipIpcGetMemHandle";
351 case HIP_API_ID_hipMemcpyHtoDAsync:
return "hipMemcpyHtoDAsync";
352 case HIP_API_ID_hipCtxGetDevice:
return "hipCtxGetDevice";
353 case HIP_API_ID_hipMemset3D:
return "hipMemset3D";
354 case HIP_API_ID_hipModuleLoadData:
return "hipModuleLoadData";
355 case HIP_API_ID_hipDeviceTotalMem:
return "hipDeviceTotalMem";
356 case HIP_API_ID_hipOccupancyMaxActiveBlocksPerMultiprocessor:
return "hipOccupancyMaxActiveBlocksPerMultiprocessor";
357 case HIP_API_ID_hipCtxSetCurrent:
return "hipCtxSetCurrent";
358 case HIP_API_ID_hipGetErrorString:
return "hipGetErrorString";
359 case HIP_API_ID_hipDevicePrimaryCtxRetain:
return "hipDevicePrimaryCtxRetain";
360 case HIP_API_ID_hipDeviceDisablePeerAccess:
return "hipDeviceDisablePeerAccess";
361 case HIP_API_ID_hipStreamCreateWithFlags:
return "hipStreamCreateWithFlags";
362 case HIP_API_ID_hipMemcpyFromArray:
return "hipMemcpyFromArray";
363 case HIP_API_ID_hipMemcpy2DAsync:
return "hipMemcpy2DAsync";
364 case HIP_API_ID_hipFuncGetAttributes:
return "hipFuncGetAttributes";
365 case HIP_API_ID_hipGetSymbolSize:
return "hipGetSymbolSize";
366 case HIP_API_ID_hipEventCreateWithFlags:
return "hipEventCreateWithFlags";
367 case HIP_API_ID_hipStreamQuery:
return "hipStreamQuery";
368 case HIP_API_ID_hipDeviceGetPCIBusId:
return "hipDeviceGetPCIBusId";
369 case HIP_API_ID_hipMemcpy:
return "hipMemcpy";
370 case HIP_API_ID_hipPeekAtLastError:
return "hipPeekAtLastError";
371 case HIP_API_ID_hipExtLaunchMultiKernelMultiDevice:
return "hipExtLaunchMultiKernelMultiDevice";
372 case HIP_API_ID_hipStreamAddCallback:
return "hipStreamAddCallback";
373 case HIP_API_ID_hipMemcpyToArray:
return "hipMemcpyToArray";
374 case HIP_API_ID_hipMemsetD32:
return "hipMemsetD32";
375 case HIP_API_ID_hipExtModuleLaunchKernel:
return "hipExtModuleLaunchKernel";
376 case HIP_API_ID_hipDeviceSynchronize:
return "hipDeviceSynchronize";
377 case HIP_API_ID_hipDeviceGetCacheConfig:
return "hipDeviceGetCacheConfig";
378 case HIP_API_ID_hipMalloc3D:
return "hipMalloc3D";
379 case HIP_API_ID_hipPointerGetAttributes:
return "hipPointerGetAttributes";
380 case HIP_API_ID_hipMemsetAsync:
return "hipMemsetAsync";
381 case HIP_API_ID_hipMemcpyToSymbol:
return "hipMemcpyToSymbol";
382 case HIP_API_ID_hipCtxPushCurrent:
return "hipCtxPushCurrent";
383 case HIP_API_ID_hipMemcpyPeer:
return "hipMemcpyPeer";
384 case HIP_API_ID_hipEventSynchronize:
return "hipEventSynchronize";
385 case HIP_API_ID_hipMemcpyDtoDAsync:
return "hipMemcpyDtoDAsync";
386 case HIP_API_ID_hipExtMallocWithFlags:
return "hipExtMallocWithFlags";
387 case HIP_API_ID_hipCtxEnablePeerAccess:
return "hipCtxEnablePeerAccess";
388 case HIP_API_ID_hipMemcpyDtoHAsync:
return "hipMemcpyDtoHAsync";
389 case HIP_API_ID_hipModuleLaunchKernel:
return "hipModuleLaunchKernel";
390 case HIP_API_ID_hipMemAllocPitch:
return "hipMemAllocPitch";
391 case HIP_API_ID_hipMemcpy2DFromArrayAsync:
return "hipMemcpy2DFromArrayAsync";
392 case HIP_API_ID_hipDeviceGetLimit:
return "hipDeviceGetLimit";
393 case HIP_API_ID_hipModuleLoadDataEx:
return "hipModuleLoadDataEx";
394 case HIP_API_ID_hipRuntimeGetVersion:
return "hipRuntimeGetVersion";
395 case HIP_API_ID___hipPopCallConfiguration:
return "__hipPopCallConfiguration";
396 case HIP_API_ID_hipGetDeviceProperties:
return "hipGetDeviceProperties";
397 case HIP_API_ID_hipFreeArray:
return "hipFreeArray";
398 case HIP_API_ID_hipEventElapsedTime:
return "hipEventElapsedTime";
399 case HIP_API_ID_hipDevicePrimaryCtxRelease:
return "hipDevicePrimaryCtxRelease";
400 case HIP_API_ID_hipHostGetDevicePointer:
return "hipHostGetDevicePointer";
401 case HIP_API_ID_hipMemcpyParam2D:
return "hipMemcpyParam2D";
402 case HIP_API_ID_hipModuleGetFunction:
return "hipModuleGetFunction";
403 case HIP_API_ID_hipMemsetD32Async:
return "hipMemsetD32Async";
404 case HIP_API_ID_hipGetDevice:
return "hipGetDevice";
405 case HIP_API_ID_hipGetDeviceCount:
return "hipGetDeviceCount";
412 uint64_t correlation_id;
419 } hipStreamCreateWithPriority;
421 const void* symbolName;
427 } hipMemcpyToSymbolAsync;
440 unsigned short value;
456 size_t dynSharedMemPerBlk;
457 } hipDrvOccupancyMaxActiveBlocksPerMultiprocessor;
464 } hipCtxGetApiVersion;
472 const void* symbolName;
477 } hipMemcpyFromSymbolAsync;
481 unsigned int* linktype;
482 unsigned int* hopcount;
483 } hipExtGetLinkTypeAndHopCount;
501 } hipMemcpy2DToArray;
510 } hipCtxGetCacheConfig;
515 } hipStreamWaitEvent;
518 int* greatestPriority;
519 } hipDeviceGetStreamPriorityRange;
527 } hipDevicePrimaryCtxSetFlags;
533 unsigned int sharedMemBytes;
535 } hipLaunchCooperativeKernel;
540 } hipLaunchCooperativeKernelMultiDevice;
564 } hipDevicePrimaryCtxGetState;
572 size_t dynSharedMemPerBlk;
574 } hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags;
579 hipDeviceptr_t* pbase;
582 } hipMemGetAddressRange;
585 const void* symbolName;
589 } hipMemcpyFromSymbol;
607 } hipCtxGetSharedMemConfig;
614 hipFunction_attribute attrib;
616 } hipFuncGetAttribute;
628 } __hipPushCallConfiguration;
650 } hipStreamGetPriority;
670 } hipDeviceCanAccessPeer;
674 } hipDeviceEnablePeerAccess;
676 const void* function_address;
680 size_t sharedMemBytes;
685 unsigned short value;
700 } hipStreamSynchronize;
703 } hipDeviceSetCacheConfig;
705 hipError_t hip_error;
713 hipDeviceptr_t* dptr;
717 } hipModuleGetGlobal;
740 } hipIpcCloseMemHandle;
749 } hipDeviceComputeCapability;
756 } hipCtxSetCacheConfig;
760 } hipFuncSetCacheConfig;
765 } hipModuleGetTexRef;
773 } hipMemcpyPeerAsync;
780 } hipMemcpyWithStream;
783 } hipDevicePrimaryCtxReset;
796 const void* symbolName;
797 } hipGetSymbolAddress;
799 unsigned int* flagsPtr;
809 } hipDriverGetVersion;
827 } hipMemcpyParam2DAsync;
835 } hipCtxSetSharedMemConfig;
844 } hipIpcOpenMemHandle;
847 } hipDeviceSetSharedMemConfig;
853 } hipDeviceGetSharedMemConfig;
863 } hipMemcpy2DFromArray;
865 unsigned int* numBlocks;
867 unsigned int blockSize;
868 size_t dynSharedMemPerBlk;
870 } hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags;
876 unsigned int globalWorkSizeX;
877 unsigned int globalWorkSizeY;
878 unsigned int globalWorkSizeZ;
879 unsigned int localWorkSizeX;
880 unsigned int localWorkSizeY;
881 unsigned int localWorkSizeZ;
882 size_t sharedMemBytes;
888 } hipHccModuleLaunchKernel;
893 unsigned int* gridSize;
894 unsigned int* blockSize;
896 size_t dynSharedMemPerBlk;
897 unsigned int blockSizeLimit;
898 } hipOccupancyMaxPotentialBlockSize;
903 } hipDeviceGetAttribute;
911 } hipCtxDisablePeerAccess;
919 const char* pciBusId;
920 } hipDeviceGetByPCIBusId;
924 } hipIpcGetMemHandle;
930 } hipMemcpyHtoDAsync;
948 unsigned int* numBlocks;
950 unsigned int blockSize;
951 size_t dynSharedMemPerBlk;
952 } hipOccupancyMaxActiveBlocksPerMultiprocessor;
962 } hipDevicePrimaryCtxRetain;
965 } hipDeviceDisablePeerAccess;
969 } hipStreamCreateWithFlags;
977 } hipMemcpyFromArray;
991 } hipFuncGetAttributes;
994 const void* symbolName;
999 } hipEventCreateWithFlags;
1007 } hipDeviceGetPCIBusId;
1018 } hipExtLaunchMultiKernelMultiDevice;
1024 } hipStreamAddCallback;
1034 hipDeviceptr_t dest;
1040 unsigned int globalWorkSizeX;
1041 unsigned int globalWorkSizeY;
1042 unsigned int globalWorkSizeZ;
1043 unsigned int localWorkSizeX;
1044 unsigned int localWorkSizeY;
1045 unsigned int localWorkSizeZ;
1046 size_t sharedMemBytes;
1048 void** kernelParams;
1053 } hipExtModuleLaunchKernel;
1056 } hipDeviceGetCacheConfig;
1064 } hipPointerGetAttributes;
1072 const void* symbolName;
1077 } hipMemcpyToSymbol;
1080 } hipCtxPushCurrent;
1090 } hipEventSynchronize;
1096 } hipMemcpyDtoDAsync;
1101 } hipExtMallocWithFlags;
1105 } hipCtxEnablePeerAccess;
1111 } hipMemcpyDtoHAsync;
1114 unsigned int gridDimX;
1115 unsigned int gridDimY;
1116 unsigned int gridDimZ;
1117 unsigned int blockDimX;
1118 unsigned int blockDimY;
1119 unsigned int blockDimZ;
1120 unsigned int sharedMemBytes;
1122 void** kernelParams;
1124 } hipModuleLaunchKernel;
1126 hipDeviceptr_t* dptr;
1128 size_t widthInBytes;
1130 unsigned int elementSizeBytes;
1142 } hipMemcpy2DFromArrayAsync;
1145 enum hipLimit_t limit;
1146 } hipDeviceGetLimit;
1150 unsigned int numOptions;
1151 hipJitOption* options;
1152 void** optionValues;
1153 } hipModuleLoadDataEx;
1155 int* runtimeVersion;
1156 } hipRuntimeGetVersion;
1162 } __hipPopCallConfiguration;
1166 } hipGetDeviceProperties;
1174 } hipEventElapsedTime;
1177 } hipDevicePrimaryCtxRelease;
1182 } hipHostGetDevicePointer;
1190 } hipModuleGetFunction;
1196 } hipMemsetD32Async;
1202 } hipGetDeviceCount;
1208 #define INIT_hipStreamCreateWithPriority_CB_ARGS_DATA(cb_data) { \ 1209 cb_data.args.hipStreamCreateWithPriority.stream = stream; \ 1210 cb_data.args.hipStreamCreateWithPriority.flags = flags; \ 1211 cb_data.args.hipStreamCreateWithPriority.priority = priority; \ 1214 #define INIT_hipMemcpyToSymbolAsync_CB_ARGS_DATA(cb_data) { \ 1217 #define INIT_hipMallocPitch_CB_ARGS_DATA(cb_data) { \ 1218 cb_data.args.hipMallocPitch.ptr = ptr; \ 1219 cb_data.args.hipMallocPitch.pitch = pitch; \ 1220 cb_data.args.hipMallocPitch.width = width; \ 1221 cb_data.args.hipMallocPitch.height = height; \ 1224 #define INIT_hipMalloc_CB_ARGS_DATA(cb_data) { \ 1225 cb_data.args.hipMalloc.ptr = ptr; \ 1226 cb_data.args.hipMalloc.size = sizeBytes; \ 1229 #define INIT_hipMemsetD16_CB_ARGS_DATA(cb_data) { \ 1230 cb_data.args.hipMemsetD16.dest = dst; \ 1231 cb_data.args.hipMemsetD16.value = value; \ 1232 cb_data.args.hipMemsetD16.count = count; \ 1235 #define INIT_hipDeviceGetName_CB_ARGS_DATA(cb_data) { \ 1236 cb_data.args.hipDeviceGetName.name = name; \ 1237 cb_data.args.hipDeviceGetName.len = len; \ 1238 cb_data.args.hipDeviceGetName.device = device; \ 1241 #define INIT_hipEventRecord_CB_ARGS_DATA(cb_data) { \ 1242 cb_data.args.hipEventRecord.event = event; \ 1243 cb_data.args.hipEventRecord.stream = stream; \ 1246 #define INIT_hipCtxSynchronize_CB_ARGS_DATA(cb_data) { \ 1249 #define INIT_hipDrvOccupancyMaxActiveBlocksPerMultiprocessor_CB_ARGS_DATA(cb_data) { \ 1250 cb_data.args.hipDrvOccupancyMaxActiveBlocksPerMultiprocessor.numBlocks = numBlocks; \ 1251 cb_data.args.hipDrvOccupancyMaxActiveBlocksPerMultiprocessor.f = f; \ 1252 cb_data.args.hipDrvOccupancyMaxActiveBlocksPerMultiprocessor.blockSize = blockSize; \ 1253 cb_data.args.hipDrvOccupancyMaxActiveBlocksPerMultiprocessor.dynSharedMemPerBlk = dynSharedMemPerBlk; \ 1256 #define INIT_hipSetDevice_CB_ARGS_DATA(cb_data) { \ 1257 cb_data.args.hipSetDevice.deviceId = deviceId; \ 1260 #define INIT_hipCtxGetApiVersion_CB_ARGS_DATA(cb_data) { \ 1261 cb_data.args.hipCtxGetApiVersion.ctx = ctx; \ 1262 cb_data.args.hipCtxGetApiVersion.apiVersion = apiVersion; \ 1265 #define INIT_hipSetupArgument_CB_ARGS_DATA(cb_data) { \ 1266 cb_data.args.hipSetupArgument.arg = arg; \ 1267 cb_data.args.hipSetupArgument.size = size; \ 1268 cb_data.args.hipSetupArgument.offset = offset; \ 1271 #define INIT_hipMemcpyFromSymbolAsync_CB_ARGS_DATA(cb_data) { \ 1274 #define INIT_hipExtGetLinkTypeAndHopCount_CB_ARGS_DATA(cb_data) { \ 1275 cb_data.args.hipExtGetLinkTypeAndHopCount.device1 = device1; \ 1276 cb_data.args.hipExtGetLinkTypeAndHopCount.device2 = device2; \ 1277 cb_data.args.hipExtGetLinkTypeAndHopCount.linktype = linktype; \ 1278 cb_data.args.hipExtGetLinkTypeAndHopCount.hopcount = hopcount; \ 1281 #define INIT_hipMemcpyDtoD_CB_ARGS_DATA(cb_data) { \ 1282 cb_data.args.hipMemcpyDtoD.dst = dst; \ 1283 cb_data.args.hipMemcpyDtoD.src = src; \ 1284 cb_data.args.hipMemcpyDtoD.sizeBytes = sizeBytes; \ 1287 #define INIT_hipHostFree_CB_ARGS_DATA(cb_data) { \ 1288 cb_data.args.hipHostFree.ptr = ptr; \ 1291 #define INIT_hipMemcpy2DToArray_CB_ARGS_DATA(cb_data) { \ 1292 cb_data.args.hipMemcpy2DToArray.dst = dst; \ 1293 cb_data.args.hipMemcpy2DToArray.wOffset = wOffset; \ 1294 cb_data.args.hipMemcpy2DToArray.hOffset = hOffset; \ 1295 cb_data.args.hipMemcpy2DToArray.src = src; \ 1296 cb_data.args.hipMemcpy2DToArray.spitch = spitch; \ 1297 cb_data.args.hipMemcpy2DToArray.width = width; \ 1298 cb_data.args.hipMemcpy2DToArray.height = height; \ 1299 cb_data.args.hipMemcpy2DToArray.kind = kind; \ 1302 #define INIT_hipMemsetD8Async_CB_ARGS_DATA(cb_data) { \ 1303 cb_data.args.hipMemsetD8Async.dest = dst; \ 1304 cb_data.args.hipMemsetD8Async.value = value; \ 1305 cb_data.args.hipMemsetD8Async.count = count; \ 1306 cb_data.args.hipMemsetD8Async.stream = stream; \ 1309 #define INIT_hipCtxGetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1310 cb_data.args.hipCtxGetCacheConfig.cacheConfig = cacheConfig; \ 1313 #define INIT_hipStreamWaitEvent_CB_ARGS_DATA(cb_data) { \ 1314 cb_data.args.hipStreamWaitEvent.stream = stream; \ 1315 cb_data.args.hipStreamWaitEvent.event = event; \ 1316 cb_data.args.hipStreamWaitEvent.flags = flags; \ 1319 #define INIT_hipDeviceGetStreamPriorityRange_CB_ARGS_DATA(cb_data) { \ 1320 cb_data.args.hipDeviceGetStreamPriorityRange.leastPriority = leastPriority; \ 1321 cb_data.args.hipDeviceGetStreamPriorityRange.greatestPriority = greatestPriority; \ 1324 #define INIT_hipModuleLoad_CB_ARGS_DATA(cb_data) { \ 1325 cb_data.args.hipModuleLoad.module = module; \ 1326 cb_data.args.hipModuleLoad.fname = fname; \ 1329 #define INIT_hipDevicePrimaryCtxSetFlags_CB_ARGS_DATA(cb_data) { \ 1330 cb_data.args.hipDevicePrimaryCtxSetFlags.dev = dev; \ 1331 cb_data.args.hipDevicePrimaryCtxSetFlags.flags = flags; \ 1334 #define INIT_hipLaunchCooperativeKernel_CB_ARGS_DATA(cb_data) { \ 1337 #define INIT_hipLaunchCooperativeKernelMultiDevice_CB_ARGS_DATA(cb_data) { \ 1340 #define INIT_hipMemcpyAsync_CB_ARGS_DATA(cb_data) { \ 1341 cb_data.args.hipMemcpyAsync.dst = dst; \ 1342 cb_data.args.hipMemcpyAsync.src = src; \ 1343 cb_data.args.hipMemcpyAsync.sizeBytes = sizeBytes; \ 1344 cb_data.args.hipMemcpyAsync.kind = kind; \ 1345 cb_data.args.hipMemcpyAsync.stream = stream; \ 1348 #define INIT_hipMalloc3DArray_CB_ARGS_DATA(cb_data) { \ 1349 cb_data.args.hipMalloc3DArray.array = array; \ 1350 cb_data.args.hipMalloc3DArray.desc = desc; \ 1351 cb_data.args.hipMalloc3DArray.extent = extent; \ 1352 cb_data.args.hipMalloc3DArray.flags = flags; \ 1355 #define INIT_hipStreamCreate_CB_ARGS_DATA(cb_data) { \ 1356 cb_data.args.hipStreamCreate.stream = stream; \ 1359 #define INIT_hipCtxGetCurrent_CB_ARGS_DATA(cb_data) { \ 1360 cb_data.args.hipCtxGetCurrent.ctx = ctx; \ 1363 #define INIT_hipDevicePrimaryCtxGetState_CB_ARGS_DATA(cb_data) { \ 1364 cb_data.args.hipDevicePrimaryCtxGetState.dev = dev; \ 1365 cb_data.args.hipDevicePrimaryCtxGetState.flags = flags; \ 1366 cb_data.args.hipDevicePrimaryCtxGetState.active = active; \ 1369 #define INIT_hipEventQuery_CB_ARGS_DATA(cb_data) { \ 1370 cb_data.args.hipEventQuery.event = event; \ 1373 #define INIT_hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags_CB_ARGS_DATA(cb_data) { \ 1374 cb_data.args.hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.numBlocks = numBlocks; \ 1375 cb_data.args.hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.f = f; \ 1376 cb_data.args.hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.blockSize = blockSize; \ 1377 cb_data.args.hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.dynSharedMemPerBlk = dynSharedMemPerBlk; \ 1378 cb_data.args.hipDrvOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.flags = flags; \ 1381 #define INIT_hipEventCreate_CB_ARGS_DATA(cb_data) { \ 1382 cb_data.args.hipEventCreate.event = event; \ 1385 #define INIT_hipMemGetAddressRange_CB_ARGS_DATA(cb_data) { \ 1386 cb_data.args.hipMemGetAddressRange.pbase = pbase; \ 1387 cb_data.args.hipMemGetAddressRange.psize = psize; \ 1388 cb_data.args.hipMemGetAddressRange.dptr = dptr; \ 1391 #define INIT_hipMemcpyFromSymbol_CB_ARGS_DATA(cb_data) { \ 1394 #define INIT_hipArrayCreate_CB_ARGS_DATA(cb_data) { \ 1395 cb_data.args.hipArrayCreate.pHandle = array; \ 1396 cb_data.args.hipArrayCreate.pAllocateArray = pAllocateArray; \ 1399 #define INIT_hipStreamGetFlags_CB_ARGS_DATA(cb_data) { \ 1400 cb_data.args.hipStreamGetFlags.stream = stream; \ 1401 cb_data.args.hipStreamGetFlags.flags = flags; \ 1404 #define INIT_hipMallocArray_CB_ARGS_DATA(cb_data) { \ 1405 cb_data.args.hipMallocArray.array = array; \ 1406 cb_data.args.hipMallocArray.desc = desc; \ 1407 cb_data.args.hipMallocArray.width = width; \ 1408 cb_data.args.hipMallocArray.height = height; \ 1409 cb_data.args.hipMallocArray.flags = flags; \ 1412 #define INIT_hipCtxGetSharedMemConfig_CB_ARGS_DATA(cb_data) { \ 1413 cb_data.args.hipCtxGetSharedMemConfig.pConfig = pConfig; \ 1416 #define INIT_hipMemPtrGetInfo_CB_ARGS_DATA(cb_data) { \ 1417 cb_data.args.hipMemPtrGetInfo.ptr = ptr; \ 1418 cb_data.args.hipMemPtrGetInfo.size = size; \ 1421 #define INIT_hipFuncGetAttribute_CB_ARGS_DATA(cb_data) { \ 1422 cb_data.args.hipFuncGetAttribute.value = value; \ 1423 cb_data.args.hipFuncGetAttribute.attrib = attrib; \ 1424 cb_data.args.hipFuncGetAttribute.hfunc = hfunc; \ 1427 #define INIT_hipCtxGetFlags_CB_ARGS_DATA(cb_data) { \ 1428 cb_data.args.hipCtxGetFlags.flags = flags; \ 1431 #define INIT_hipStreamDestroy_CB_ARGS_DATA(cb_data) { \ 1432 cb_data.args.hipStreamDestroy.stream = stream; \ 1435 #define INIT___hipPushCallConfiguration_CB_ARGS_DATA(cb_data) { \ 1438 #define INIT_hipMemset3DAsync_CB_ARGS_DATA(cb_data) { \ 1439 cb_data.args.hipMemset3DAsync.pitchedDevPtr = pitchedDevPtr; \ 1440 cb_data.args.hipMemset3DAsync.value = value; \ 1441 cb_data.args.hipMemset3DAsync.extent = extent; \ 1442 cb_data.args.hipMemset3DAsync.stream = stream; \ 1445 #define INIT_hipMemcpy3D_CB_ARGS_DATA(cb_data) { \ 1446 cb_data.args.hipMemcpy3D.p = p; \ 1449 #define INIT_hipInit_CB_ARGS_DATA(cb_data) { \ 1450 cb_data.args.hipInit.flags = flags; \ 1453 #define INIT_hipMemcpyAtoH_CB_ARGS_DATA(cb_data) { \ 1454 cb_data.args.hipMemcpyAtoH.dst = dst; \ 1455 cb_data.args.hipMemcpyAtoH.srcArray = srcArray; \ 1456 cb_data.args.hipMemcpyAtoH.srcOffset = srcOffset; \ 1457 cb_data.args.hipMemcpyAtoH.count = count; \ 1460 #define INIT_hipStreamGetPriority_CB_ARGS_DATA(cb_data) { \ 1461 cb_data.args.hipStreamGetPriority.stream = stream; \ 1462 cb_data.args.hipStreamGetPriority.priority = priority; \ 1465 #define INIT_hipMemset2D_CB_ARGS_DATA(cb_data) { \ 1466 cb_data.args.hipMemset2D.dst = dst; \ 1467 cb_data.args.hipMemset2D.pitch = pitch; \ 1468 cb_data.args.hipMemset2D.value = value; \ 1469 cb_data.args.hipMemset2D.width = width; \ 1470 cb_data.args.hipMemset2D.height = height; \ 1473 #define INIT_hipMemset2DAsync_CB_ARGS_DATA(cb_data) { \ 1474 cb_data.args.hipMemset2DAsync.dst = dst; \ 1475 cb_data.args.hipMemset2DAsync.pitch = pitch; \ 1476 cb_data.args.hipMemset2DAsync.value = value; \ 1477 cb_data.args.hipMemset2DAsync.width = width; \ 1478 cb_data.args.hipMemset2DAsync.height = height; \ 1479 cb_data.args.hipMemset2DAsync.stream = stream; \ 1482 #define INIT_hipDeviceCanAccessPeer_CB_ARGS_DATA(cb_data) { \ 1483 cb_data.args.hipDeviceCanAccessPeer.canAccessPeer = canAccessPeer; \ 1484 cb_data.args.hipDeviceCanAccessPeer.deviceId = deviceId; \ 1485 cb_data.args.hipDeviceCanAccessPeer.peerDeviceId = peerDeviceId; \ 1488 #define INIT_hipDeviceEnablePeerAccess_CB_ARGS_DATA(cb_data) { \ 1489 cb_data.args.hipDeviceEnablePeerAccess.peerDeviceId = peerDeviceId; \ 1490 cb_data.args.hipDeviceEnablePeerAccess.flags = flags; \ 1493 #define INIT_hipLaunchKernel_CB_ARGS_DATA(cb_data) { \ 1494 cb_data.args.hipLaunchKernel.function_address = func_addr; \ 1495 cb_data.args.hipLaunchKernel.numBlocks = numBlocks; \ 1496 cb_data.args.hipLaunchKernel.dimBlocks = dimBlocks; \ 1497 cb_data.args.hipLaunchKernel.args = args; \ 1498 cb_data.args.hipLaunchKernel.sharedMemBytes = sharedMemBytes; \ 1499 cb_data.args.hipLaunchKernel.stream = stream; \ 1502 #define INIT_hipMemsetD16Async_CB_ARGS_DATA(cb_data) { \ 1503 cb_data.args.hipMemsetD16Async.dest = dst; \ 1504 cb_data.args.hipMemsetD16Async.value = value; \ 1505 cb_data.args.hipMemsetD16Async.count = count; \ 1506 cb_data.args.hipMemsetD16Async.stream = stream; \ 1509 #define INIT_hipModuleUnload_CB_ARGS_DATA(cb_data) { \ 1510 cb_data.args.hipModuleUnload.module = hmod; \ 1513 #define INIT_hipHostUnregister_CB_ARGS_DATA(cb_data) { \ 1514 cb_data.args.hipHostUnregister.hostPtr = hostPtr; \ 1517 #define INIT_hipProfilerStop_CB_ARGS_DATA(cb_data) { \ 1520 #define INIT_hipLaunchByPtr_CB_ARGS_DATA(cb_data) { \ 1521 cb_data.args.hipLaunchByPtr.func = hostFunction; \ 1524 #define INIT_hipStreamSynchronize_CB_ARGS_DATA(cb_data) { \ 1525 cb_data.args.hipStreamSynchronize.stream = stream; \ 1528 #define INIT_hipDeviceSetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1529 cb_data.args.hipDeviceSetCacheConfig.cacheConfig = cacheConfig; \ 1532 #define INIT_hipGetErrorName_CB_ARGS_DATA(cb_data) { \ 1533 cb_data.args.hipGetErrorName.hip_error = hip_error; \ 1536 #define INIT_hipMemcpyHtoD_CB_ARGS_DATA(cb_data) { \ 1537 cb_data.args.hipMemcpyHtoD.dst = dst; \ 1538 cb_data.args.hipMemcpyHtoD.src = src; \ 1539 cb_data.args.hipMemcpyHtoD.sizeBytes = sizeBytes; \ 1542 #define INIT_hipModuleGetGlobal_CB_ARGS_DATA(cb_data) { \ 1543 cb_data.args.hipModuleGetGlobal.dptr = dptr; \ 1544 cb_data.args.hipModuleGetGlobal.bytes = bytes; \ 1545 cb_data.args.hipModuleGetGlobal.hmod = hmod; \ 1546 cb_data.args.hipModuleGetGlobal.name = name; \ 1549 #define INIT_hipMemcpyHtoA_CB_ARGS_DATA(cb_data) { \ 1550 cb_data.args.hipMemcpyHtoA.dstArray = dstArray; \ 1551 cb_data.args.hipMemcpyHtoA.dstOffset = dstOffset; \ 1552 cb_data.args.hipMemcpyHtoA.srcHost = srcHost; \ 1553 cb_data.args.hipMemcpyHtoA.count = count; \ 1556 #define INIT_hipCtxCreate_CB_ARGS_DATA(cb_data) { \ 1557 cb_data.args.hipCtxCreate.ctx = ctx; \ 1558 cb_data.args.hipCtxCreate.flags = flags; \ 1559 cb_data.args.hipCtxCreate.device = device; \ 1562 #define INIT_hipMemcpy2D_CB_ARGS_DATA(cb_data) { \ 1563 cb_data.args.hipMemcpy2D.dst = dst; \ 1564 cb_data.args.hipMemcpy2D.dpitch = dpitch; \ 1565 cb_data.args.hipMemcpy2D.src = src; \ 1566 cb_data.args.hipMemcpy2D.spitch = spitch; \ 1567 cb_data.args.hipMemcpy2D.width = width; \ 1568 cb_data.args.hipMemcpy2D.height = height; \ 1569 cb_data.args.hipMemcpy2D.kind = kind; \ 1572 #define INIT_hipIpcCloseMemHandle_CB_ARGS_DATA(cb_data) { \ 1573 cb_data.args.hipIpcCloseMemHandle.devPtr = devPtr; \ 1576 #define INIT_hipChooseDevice_CB_ARGS_DATA(cb_data) { \ 1577 cb_data.args.hipChooseDevice.device = device; \ 1578 cb_data.args.hipChooseDevice.prop = prop; \ 1581 #define INIT_hipGetLastError_CB_ARGS_DATA(cb_data) { \ 1584 #define INIT_hipDeviceComputeCapability_CB_ARGS_DATA(cb_data) { \ 1585 cb_data.args.hipDeviceComputeCapability.major = major; \ 1586 cb_data.args.hipDeviceComputeCapability.minor = minor; \ 1587 cb_data.args.hipDeviceComputeCapability.device = device; \ 1590 #define INIT_hipDeviceGet_CB_ARGS_DATA(cb_data) { \ 1591 cb_data.args.hipDeviceGet.device = device; \ 1592 cb_data.args.hipDeviceGet.ordinal = deviceId; \ 1595 #define INIT_hipProfilerStart_CB_ARGS_DATA(cb_data) { \ 1598 #define INIT_hipCtxSetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1599 cb_data.args.hipCtxSetCacheConfig.cacheConfig = cacheConfig; \ 1602 #define INIT_hipFuncSetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1603 cb_data.args.hipFuncSetCacheConfig.func = func; \ 1604 cb_data.args.hipFuncSetCacheConfig.config = cacheConfig; \ 1607 #define INIT_hipModuleGetTexRef_CB_ARGS_DATA(cb_data) { \ 1608 cb_data.args.hipModuleGetTexRef.texRef = texRef; \ 1609 cb_data.args.hipModuleGetTexRef.hmod = hmod; \ 1610 cb_data.args.hipModuleGetTexRef.name = name; \ 1613 #define INIT_hipMemcpyPeerAsync_CB_ARGS_DATA(cb_data) { \ 1614 cb_data.args.hipMemcpyPeerAsync.dst = dst; \ 1615 cb_data.args.hipMemcpyPeerAsync.dstDeviceId = dstDevice; \ 1616 cb_data.args.hipMemcpyPeerAsync.src = src; \ 1617 cb_data.args.hipMemcpyPeerAsync.srcDevice = srcDevice; \ 1618 cb_data.args.hipMemcpyPeerAsync.sizeBytes = sizeBytes; \ 1619 cb_data.args.hipMemcpyPeerAsync.stream = stream; \ 1622 #define INIT_hipMemcpyWithStream_CB_ARGS_DATA(cb_data) { \ 1623 cb_data.args.hipMemcpyWithStream.dst = dst; \ 1624 cb_data.args.hipMemcpyWithStream.src = src; \ 1625 cb_data.args.hipMemcpyWithStream.sizeBytes = sizeBytes; \ 1626 cb_data.args.hipMemcpyWithStream.kind = kind; \ 1627 cb_data.args.hipMemcpyWithStream.stream = stream; \ 1630 #define INIT_hipDevicePrimaryCtxReset_CB_ARGS_DATA(cb_data) { \ 1631 cb_data.args.hipDevicePrimaryCtxReset.dev = dev; \ 1634 #define INIT_hipMemcpy3DAsync_CB_ARGS_DATA(cb_data) { \ 1635 cb_data.args.hipMemcpy3DAsync.p = p; \ 1636 cb_data.args.hipMemcpy3DAsync.stream = stream; \ 1639 #define INIT_hipEventDestroy_CB_ARGS_DATA(cb_data) { \ 1640 cb_data.args.hipEventDestroy.event = event; \ 1643 #define INIT_hipCtxPopCurrent_CB_ARGS_DATA(cb_data) { \ 1644 cb_data.args.hipCtxPopCurrent.ctx = ctx; \ 1647 #define INIT_hipGetSymbolAddress_CB_ARGS_DATA(cb_data) { \ 1650 #define INIT_hipHostGetFlags_CB_ARGS_DATA(cb_data) { \ 1651 cb_data.args.hipHostGetFlags.flagsPtr = flagsPtr; \ 1652 cb_data.args.hipHostGetFlags.hostPtr = hostPtr; \ 1655 #define INIT_hipHostMalloc_CB_ARGS_DATA(cb_data) { \ 1656 cb_data.args.hipHostMalloc.ptr = ptr; \ 1657 cb_data.args.hipHostMalloc.size = sizeBytes; \ 1658 cb_data.args.hipHostMalloc.flags = flags; \ 1661 #define INIT_hipDriverGetVersion_CB_ARGS_DATA(cb_data) { \ 1662 cb_data.args.hipDriverGetVersion.driverVersion = driverVersion; \ 1665 #define INIT_hipMemGetInfo_CB_ARGS_DATA(cb_data) { \ 1666 cb_data.args.hipMemGetInfo.free = free; \ 1667 cb_data.args.hipMemGetInfo.total = total; \ 1670 #define INIT_hipDeviceReset_CB_ARGS_DATA(cb_data) { \ 1673 #define INIT_hipMemset_CB_ARGS_DATA(cb_data) { \ 1674 cb_data.args.hipMemset.dst = dst; \ 1675 cb_data.args.hipMemset.value = value; \ 1676 cb_data.args.hipMemset.sizeBytes = sizeBytes; \ 1679 #define INIT_hipMemsetD8_CB_ARGS_DATA(cb_data) { \ 1680 cb_data.args.hipMemsetD8.dest = dst; \ 1681 cb_data.args.hipMemsetD8.value = value; \ 1682 cb_data.args.hipMemsetD8.count = count; \ 1685 #define INIT_hipMemcpyParam2DAsync_CB_ARGS_DATA(cb_data) { \ 1686 cb_data.args.hipMemcpyParam2DAsync.pCopy = pCopy; \ 1687 cb_data.args.hipMemcpyParam2DAsync.stream = stream; \ 1690 #define INIT_hipHostRegister_CB_ARGS_DATA(cb_data) { \ 1691 cb_data.args.hipHostRegister.hostPtr = hostPtr; \ 1692 cb_data.args.hipHostRegister.sizeBytes = sizeBytes; \ 1693 cb_data.args.hipHostRegister.flags = flags; \ 1696 #define INIT_hipCtxSetSharedMemConfig_CB_ARGS_DATA(cb_data) { \ 1697 cb_data.args.hipCtxSetSharedMemConfig.config = config; \ 1700 #define INIT_hipArray3DCreate_CB_ARGS_DATA(cb_data) { \ 1701 cb_data.args.hipArray3DCreate.array = array; \ 1702 cb_data.args.hipArray3DCreate.pAllocateArray = pAllocateArray; \ 1705 #define INIT_hipIpcOpenMemHandle_CB_ARGS_DATA(cb_data) { \ 1706 cb_data.args.hipIpcOpenMemHandle.devPtr = devPtr; \ 1707 cb_data.args.hipIpcOpenMemHandle.handle = handle; \ 1708 cb_data.args.hipIpcOpenMemHandle.flags = flags; \ 1711 #define INIT_hipDeviceSetSharedMemConfig_CB_ARGS_DATA(cb_data) { \ 1712 cb_data.args.hipDeviceSetSharedMemConfig.config = config; \ 1715 #define INIT_hipCtxDestroy_CB_ARGS_DATA(cb_data) { \ 1716 cb_data.args.hipCtxDestroy.ctx = ctx; \ 1719 #define INIT_hipDeviceGetSharedMemConfig_CB_ARGS_DATA(cb_data) { \ 1720 cb_data.args.hipDeviceGetSharedMemConfig.pConfig = pConfig; \ 1723 #define INIT_hipMemcpy2DFromArray_CB_ARGS_DATA(cb_data) { \ 1724 cb_data.args.hipMemcpy2DFromArray.dst = dst; \ 1725 cb_data.args.hipMemcpy2DFromArray.dpitch = dpitch; \ 1726 cb_data.args.hipMemcpy2DFromArray.src = src; \ 1727 cb_data.args.hipMemcpy2DFromArray.wOffset = wOffset; \ 1728 cb_data.args.hipMemcpy2DFromArray.hOffset = hOffset; \ 1729 cb_data.args.hipMemcpy2DFromArray.width = width; \ 1730 cb_data.args.hipMemcpy2DFromArray.height = height; \ 1731 cb_data.args.hipMemcpy2DFromArray.kind = kind; \ 1734 #define INIT_hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags_CB_ARGS_DATA(cb_data) { \ 1735 cb_data.args.hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.numBlocks = numBlocks; \ 1736 cb_data.args.hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.f = f; \ 1737 cb_data.args.hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.blockSize = blockSize; \ 1738 cb_data.args.hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.dynSharedMemPerBlk = dynSharedMemPerBlk; \ 1739 cb_data.args.hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags.flags = flags; \ 1742 #define INIT_hipSetDeviceFlags_CB_ARGS_DATA(cb_data) { \ 1743 cb_data.args.hipSetDeviceFlags.flags = flags; \ 1746 #define INIT_hipHccModuleLaunchKernel_CB_ARGS_DATA(cb_data) { \ 1747 cb_data.args.hipHccModuleLaunchKernel.f = f; \ 1748 cb_data.args.hipHccModuleLaunchKernel.globalWorkSizeX = globalWorkSizeX; \ 1749 cb_data.args.hipHccModuleLaunchKernel.globalWorkSizeY = globalWorkSizeY; \ 1750 cb_data.args.hipHccModuleLaunchKernel.globalWorkSizeZ = globalWorkSizeZ; \ 1751 cb_data.args.hipHccModuleLaunchKernel.localWorkSizeX = localWorkSizeX; \ 1752 cb_data.args.hipHccModuleLaunchKernel.localWorkSizeY = localWorkSizeY; \ 1753 cb_data.args.hipHccModuleLaunchKernel.localWorkSizeZ = localWorkSizeZ; \ 1754 cb_data.args.hipHccModuleLaunchKernel.sharedMemBytes = sharedMemBytes; \ 1755 cb_data.args.hipHccModuleLaunchKernel.hStream = hStream; \ 1756 cb_data.args.hipHccModuleLaunchKernel.kernelParams = kernelParams; \ 1757 cb_data.args.hipHccModuleLaunchKernel.extra = extra; \ 1758 cb_data.args.hipHccModuleLaunchKernel.startEvent = startEvent; \ 1759 cb_data.args.hipHccModuleLaunchKernel.stopEvent = stopEvent; \ 1762 #define INIT_hipFree_CB_ARGS_DATA(cb_data) { \ 1763 cb_data.args.hipFree.ptr = ptr; \ 1766 #define INIT_hipOccupancyMaxPotentialBlockSize_CB_ARGS_DATA(cb_data) { \ 1767 cb_data.args.hipOccupancyMaxPotentialBlockSize.gridSize = gridSize; \ 1768 cb_data.args.hipOccupancyMaxPotentialBlockSize.blockSize = blockSize; \ 1769 cb_data.args.hipOccupancyMaxPotentialBlockSize.f = f; \ 1770 cb_data.args.hipOccupancyMaxPotentialBlockSize.dynSharedMemPerBlk = dynSharedMemPerBlk; \ 1771 cb_data.args.hipOccupancyMaxPotentialBlockSize.blockSizeLimit = blockSizeLimit; \ 1774 #define INIT_hipDeviceGetAttribute_CB_ARGS_DATA(cb_data) { \ 1775 cb_data.args.hipDeviceGetAttribute.pi = pi; \ 1776 cb_data.args.hipDeviceGetAttribute.attr = attr; \ 1777 cb_data.args.hipDeviceGetAttribute.deviceId = device; \ 1780 #define INIT_hipMemcpyDtoH_CB_ARGS_DATA(cb_data) { \ 1781 cb_data.args.hipMemcpyDtoH.dst = dst; \ 1782 cb_data.args.hipMemcpyDtoH.src = src; \ 1783 cb_data.args.hipMemcpyDtoH.sizeBytes = sizeBytes; \ 1786 #define INIT_hipCtxDisablePeerAccess_CB_ARGS_DATA(cb_data) { \ 1787 cb_data.args.hipCtxDisablePeerAccess.peerCtx = peerCtx; \ 1790 #define INIT_hipMallocManaged_CB_ARGS_DATA(cb_data) { \ 1791 cb_data.args.hipMallocManaged.devPtr = devPtr; \ 1792 cb_data.args.hipMallocManaged.size = size; \ 1793 cb_data.args.hipMallocManaged.flags = flags; \ 1796 #define INIT_hipDeviceGetByPCIBusId_CB_ARGS_DATA(cb_data) { \ 1797 cb_data.args.hipDeviceGetByPCIBusId.device = device; \ 1798 cb_data.args.hipDeviceGetByPCIBusId.pciBusId = pciBusId; \ 1801 #define INIT_hipIpcGetMemHandle_CB_ARGS_DATA(cb_data) { \ 1802 cb_data.args.hipIpcGetMemHandle.handle = handle; \ 1803 cb_data.args.hipIpcGetMemHandle.devPtr = devPtr; \ 1806 #define INIT_hipMemcpyHtoDAsync_CB_ARGS_DATA(cb_data) { \ 1807 cb_data.args.hipMemcpyHtoDAsync.dst = dst; \ 1808 cb_data.args.hipMemcpyHtoDAsync.src = src; \ 1809 cb_data.args.hipMemcpyHtoDAsync.sizeBytes = sizeBytes; \ 1810 cb_data.args.hipMemcpyHtoDAsync.stream = stream; \ 1813 #define INIT_hipCtxGetDevice_CB_ARGS_DATA(cb_data) { \ 1814 cb_data.args.hipCtxGetDevice.device = device; \ 1817 #define INIT_hipMemset3D_CB_ARGS_DATA(cb_data) { \ 1818 cb_data.args.hipMemset3D.pitchedDevPtr = pitchedDevPtr; \ 1819 cb_data.args.hipMemset3D.value = value; \ 1820 cb_data.args.hipMemset3D.extent = extent; \ 1823 #define INIT_hipModuleLoadData_CB_ARGS_DATA(cb_data) { \ 1824 cb_data.args.hipModuleLoadData.module = module; \ 1825 cb_data.args.hipModuleLoadData.image = image; \ 1828 #define INIT_hipDeviceTotalMem_CB_ARGS_DATA(cb_data) { \ 1829 cb_data.args.hipDeviceTotalMem.bytes = bytes; \ 1830 cb_data.args.hipDeviceTotalMem.device = device; \ 1833 #define INIT_hipOccupancyMaxActiveBlocksPerMultiprocessor_CB_ARGS_DATA(cb_data) { \ 1834 cb_data.args.hipOccupancyMaxActiveBlocksPerMultiprocessor.numBlocks = numBlocks; \ 1835 cb_data.args.hipOccupancyMaxActiveBlocksPerMultiprocessor.f = f; \ 1836 cb_data.args.hipOccupancyMaxActiveBlocksPerMultiprocessor.blockSize = blockSize; \ 1837 cb_data.args.hipOccupancyMaxActiveBlocksPerMultiprocessor.dynSharedMemPerBlk = dynSharedMemPerBlk; \ 1840 #define INIT_hipCtxSetCurrent_CB_ARGS_DATA(cb_data) { \ 1841 cb_data.args.hipCtxSetCurrent.ctx = ctx; \ 1844 #define INIT_hipGetErrorString_CB_ARGS_DATA(cb_data) { \ 1845 cb_data.args.hipGetErrorString.hipError = hip_error; \ 1848 #define INIT_hipDevicePrimaryCtxRetain_CB_ARGS_DATA(cb_data) { \ 1849 cb_data.args.hipDevicePrimaryCtxRetain.pctx = pctx; \ 1850 cb_data.args.hipDevicePrimaryCtxRetain.dev = dev; \ 1853 #define INIT_hipDeviceDisablePeerAccess_CB_ARGS_DATA(cb_data) { \ 1854 cb_data.args.hipDeviceDisablePeerAccess.peerDeviceId = peerDeviceId; \ 1857 #define INIT_hipStreamCreateWithFlags_CB_ARGS_DATA(cb_data) { \ 1858 cb_data.args.hipStreamCreateWithFlags.stream = stream; \ 1859 cb_data.args.hipStreamCreateWithFlags.flags = flags; \ 1862 #define INIT_hipMemcpyFromArray_CB_ARGS_DATA(cb_data) { \ 1863 cb_data.args.hipMemcpyFromArray.dst = dst; \ 1864 cb_data.args.hipMemcpyFromArray.srcArray = srcArray; \ 1865 cb_data.args.hipMemcpyFromArray.wOffset = wOffset; \ 1866 cb_data.args.hipMemcpyFromArray.hOffset = hOffset; \ 1867 cb_data.args.hipMemcpyFromArray.count = count; \ 1868 cb_data.args.hipMemcpyFromArray.kind = kind; \ 1871 #define INIT_hipMemcpy2DAsync_CB_ARGS_DATA(cb_data) { \ 1872 cb_data.args.hipMemcpy2DAsync.dst = dst; \ 1873 cb_data.args.hipMemcpy2DAsync.dpitch = dpitch; \ 1874 cb_data.args.hipMemcpy2DAsync.src = src; \ 1875 cb_data.args.hipMemcpy2DAsync.spitch = spitch; \ 1876 cb_data.args.hipMemcpy2DAsync.width = width; \ 1877 cb_data.args.hipMemcpy2DAsync.height = height; \ 1878 cb_data.args.hipMemcpy2DAsync.kind = kind; \ 1879 cb_data.args.hipMemcpy2DAsync.stream = stream; \ 1882 #define INIT_hipFuncGetAttributes_CB_ARGS_DATA(cb_data) { \ 1883 cb_data.args.hipFuncGetAttributes.attr = attr; \ 1884 cb_data.args.hipFuncGetAttributes.func = func; \ 1887 #define INIT_hipGetSymbolSize_CB_ARGS_DATA(cb_data) { \ 1890 #define INIT_hipEventCreateWithFlags_CB_ARGS_DATA(cb_data) { \ 1891 cb_data.args.hipEventCreateWithFlags.event = event; \ 1892 cb_data.args.hipEventCreateWithFlags.flags = flags; \ 1895 #define INIT_hipStreamQuery_CB_ARGS_DATA(cb_data) { \ 1896 cb_data.args.hipStreamQuery.stream = stream; \ 1899 #define INIT_hipDeviceGetPCIBusId_CB_ARGS_DATA(cb_data) { \ 1900 cb_data.args.hipDeviceGetPCIBusId.pciBusId = pciBusId; \ 1901 cb_data.args.hipDeviceGetPCIBusId.len = len; \ 1902 cb_data.args.hipDeviceGetPCIBusId.device = device; \ 1905 #define INIT_hipMemcpy_CB_ARGS_DATA(cb_data) { \ 1906 cb_data.args.hipMemcpy.dst = dst; \ 1907 cb_data.args.hipMemcpy.src = src; \ 1908 cb_data.args.hipMemcpy.sizeBytes = sizeBytes; \ 1909 cb_data.args.hipMemcpy.kind = kind; \ 1912 #define INIT_hipPeekAtLastError_CB_ARGS_DATA(cb_data) { \ 1915 #define INIT_hipExtLaunchMultiKernelMultiDevice_CB_ARGS_DATA(cb_data) { \ 1918 #define INIT_hipStreamAddCallback_CB_ARGS_DATA(cb_data) { \ 1919 cb_data.args.hipStreamAddCallback.stream = stream; \ 1920 cb_data.args.hipStreamAddCallback.callback = callback; \ 1921 cb_data.args.hipStreamAddCallback.userData = userData; \ 1922 cb_data.args.hipStreamAddCallback.flags = flags; \ 1925 #define INIT_hipMemcpyToArray_CB_ARGS_DATA(cb_data) { \ 1926 cb_data.args.hipMemcpyToArray.dst = dst; \ 1927 cb_data.args.hipMemcpyToArray.wOffset = wOffset; \ 1928 cb_data.args.hipMemcpyToArray.hOffset = hOffset; \ 1929 cb_data.args.hipMemcpyToArray.src = src; \ 1930 cb_data.args.hipMemcpyToArray.count = count; \ 1931 cb_data.args.hipMemcpyToArray.kind = kind; \ 1934 #define INIT_hipMemsetD32_CB_ARGS_DATA(cb_data) { \ 1935 cb_data.args.hipMemsetD32.dest = dst; \ 1936 cb_data.args.hipMemsetD32.value = value; \ 1937 cb_data.args.hipMemsetD32.count = count; \ 1940 #define INIT_hipExtModuleLaunchKernel_CB_ARGS_DATA(cb_data) { \ 1941 cb_data.args.hipExtModuleLaunchKernel.f = f; \ 1942 cb_data.args.hipExtModuleLaunchKernel.globalWorkSizeX = globalWorkSizeX; \ 1943 cb_data.args.hipExtModuleLaunchKernel.globalWorkSizeY = globalWorkSizeY; \ 1944 cb_data.args.hipExtModuleLaunchKernel.globalWorkSizeZ = globalWorkSizeZ; \ 1945 cb_data.args.hipExtModuleLaunchKernel.localWorkSizeX = localWorkSizeX; \ 1946 cb_data.args.hipExtModuleLaunchKernel.localWorkSizeY = localWorkSizeY; \ 1947 cb_data.args.hipExtModuleLaunchKernel.localWorkSizeZ = localWorkSizeZ; \ 1948 cb_data.args.hipExtModuleLaunchKernel.sharedMemBytes = sharedMemBytes; \ 1949 cb_data.args.hipExtModuleLaunchKernel.hStream = hStream; \ 1950 cb_data.args.hipExtModuleLaunchKernel.kernelParams = kernelParams; \ 1951 cb_data.args.hipExtModuleLaunchKernel.extra = extra; \ 1952 cb_data.args.hipExtModuleLaunchKernel.startEvent = startEvent; \ 1953 cb_data.args.hipExtModuleLaunchKernel.stopEvent = stopEvent; \ 1954 cb_data.args.hipExtModuleLaunchKernel.flags = flags; \ 1957 #define INIT_hipDeviceSynchronize_CB_ARGS_DATA(cb_data) { \ 1960 #define INIT_hipDeviceGetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1961 cb_data.args.hipDeviceGetCacheConfig.cacheConfig = cacheConfig; \ 1964 #define INIT_hipMalloc3D_CB_ARGS_DATA(cb_data) { \ 1965 cb_data.args.hipMalloc3D.pitchedDevPtr = pitchedDevPtr; \ 1966 cb_data.args.hipMalloc3D.extent = extent; \ 1969 #define INIT_hipPointerGetAttributes_CB_ARGS_DATA(cb_data) { \ 1970 cb_data.args.hipPointerGetAttributes.attributes = attributes; \ 1971 cb_data.args.hipPointerGetAttributes.ptr = ptr; \ 1974 #define INIT_hipMemsetAsync_CB_ARGS_DATA(cb_data) { \ 1975 cb_data.args.hipMemsetAsync.dst = dst; \ 1976 cb_data.args.hipMemsetAsync.value = value; \ 1977 cb_data.args.hipMemsetAsync.sizeBytes = sizeBytes; \ 1978 cb_data.args.hipMemsetAsync.stream = stream; \ 1981 #define INIT_hipMemcpyToSymbol_CB_ARGS_DATA(cb_data) { \ 1984 #define INIT_hipCtxPushCurrent_CB_ARGS_DATA(cb_data) { \ 1985 cb_data.args.hipCtxPushCurrent.ctx = ctx; \ 1988 #define INIT_hipMemcpyPeer_CB_ARGS_DATA(cb_data) { \ 1989 cb_data.args.hipMemcpyPeer.dst = dst; \ 1990 cb_data.args.hipMemcpyPeer.dstDeviceId = dstDevice; \ 1991 cb_data.args.hipMemcpyPeer.src = src; \ 1992 cb_data.args.hipMemcpyPeer.srcDeviceId = srcDevice; \ 1993 cb_data.args.hipMemcpyPeer.sizeBytes = sizeBytes; \ 1996 #define INIT_hipEventSynchronize_CB_ARGS_DATA(cb_data) { \ 1997 cb_data.args.hipEventSynchronize.event = event; \ 2000 #define INIT_hipMemcpyDtoDAsync_CB_ARGS_DATA(cb_data) { \ 2001 cb_data.args.hipMemcpyDtoDAsync.dst = dst; \ 2002 cb_data.args.hipMemcpyDtoDAsync.src = src; \ 2003 cb_data.args.hipMemcpyDtoDAsync.sizeBytes = sizeBytes; \ 2004 cb_data.args.hipMemcpyDtoDAsync.stream = stream; \ 2007 #define INIT_hipExtMallocWithFlags_CB_ARGS_DATA(cb_data) { \ 2008 cb_data.args.hipExtMallocWithFlags.ptr = ptr; \ 2009 cb_data.args.hipExtMallocWithFlags.sizeBytes = sizeBytes; \ 2010 cb_data.args.hipExtMallocWithFlags.flags = flags; \ 2013 #define INIT_hipCtxEnablePeerAccess_CB_ARGS_DATA(cb_data) { \ 2014 cb_data.args.hipCtxEnablePeerAccess.peerCtx = peerCtx; \ 2015 cb_data.args.hipCtxEnablePeerAccess.flags = flags; \ 2018 #define INIT_hipMemcpyDtoHAsync_CB_ARGS_DATA(cb_data) { \ 2019 cb_data.args.hipMemcpyDtoHAsync.dst = dst; \ 2020 cb_data.args.hipMemcpyDtoHAsync.src = src; \ 2021 cb_data.args.hipMemcpyDtoHAsync.sizeBytes = sizeBytes; \ 2022 cb_data.args.hipMemcpyDtoHAsync.stream = stream; \ 2025 #define INIT_hipModuleLaunchKernel_CB_ARGS_DATA(cb_data) { \ 2026 cb_data.args.hipModuleLaunchKernel.f = f; \ 2027 cb_data.args.hipModuleLaunchKernel.gridDimX = gridDimX; \ 2028 cb_data.args.hipModuleLaunchKernel.gridDimY = gridDimY; \ 2029 cb_data.args.hipModuleLaunchKernel.gridDimZ = gridDimZ; \ 2030 cb_data.args.hipModuleLaunchKernel.blockDimX = blockDimX; \ 2031 cb_data.args.hipModuleLaunchKernel.blockDimY = blockDimY; \ 2032 cb_data.args.hipModuleLaunchKernel.blockDimZ = blockDimZ; \ 2033 cb_data.args.hipModuleLaunchKernel.sharedMemBytes = sharedMemBytes; \ 2034 cb_data.args.hipModuleLaunchKernel.stream = hStream; \ 2035 cb_data.args.hipModuleLaunchKernel.kernelParams = kernelParams; \ 2036 cb_data.args.hipModuleLaunchKernel.extra = extra; \ 2039 #define INIT_hipMemAllocPitch_CB_ARGS_DATA(cb_data) { \ 2040 cb_data.args.hipMemAllocPitch.dptr = dptr; \ 2041 cb_data.args.hipMemAllocPitch.pitch = pitch; \ 2042 cb_data.args.hipMemAllocPitch.widthInBytes = widthInBytes; \ 2043 cb_data.args.hipMemAllocPitch.height = height; \ 2044 cb_data.args.hipMemAllocPitch.elementSizeBytes = elementSizeBytes; \ 2047 #define INIT_hipMemcpy2DFromArrayAsync_CB_ARGS_DATA(cb_data) { \ 2048 cb_data.args.hipMemcpy2DFromArrayAsync.dst = dst; \ 2049 cb_data.args.hipMemcpy2DFromArrayAsync.dpitch = dpitch; \ 2050 cb_data.args.hipMemcpy2DFromArrayAsync.src = src; \ 2051 cb_data.args.hipMemcpy2DFromArrayAsync.wOffset = wOffset; \ 2052 cb_data.args.hipMemcpy2DFromArrayAsync.hOffset = hOffset; \ 2053 cb_data.args.hipMemcpy2DFromArrayAsync.width = width; \ 2054 cb_data.args.hipMemcpy2DFromArrayAsync.height = height; \ 2055 cb_data.args.hipMemcpy2DFromArrayAsync.kind = kind; \ 2056 cb_data.args.hipMemcpy2DFromArrayAsync.stream = stream; \ 2059 #define INIT_hipDeviceGetLimit_CB_ARGS_DATA(cb_data) { \ 2060 cb_data.args.hipDeviceGetLimit.pValue = pValue; \ 2061 cb_data.args.hipDeviceGetLimit.limit = limit; \ 2064 #define INIT_hipModuleLoadDataEx_CB_ARGS_DATA(cb_data) { \ 2065 cb_data.args.hipModuleLoadDataEx.module = module; \ 2066 cb_data.args.hipModuleLoadDataEx.image = image; \ 2067 cb_data.args.hipModuleLoadDataEx.numOptions = numOptions; \ 2068 cb_data.args.hipModuleLoadDataEx.options = options; \ 2069 cb_data.args.hipModuleLoadDataEx.optionValues = optionValues; \ 2072 #define INIT_hipRuntimeGetVersion_CB_ARGS_DATA(cb_data) { \ 2073 cb_data.args.hipRuntimeGetVersion.runtimeVersion = runtimeVersion; \ 2076 #define INIT___hipPopCallConfiguration_CB_ARGS_DATA(cb_data) { \ 2079 #define INIT_hipGetDeviceProperties_CB_ARGS_DATA(cb_data) { \ 2080 cb_data.args.hipGetDeviceProperties.prop = props; \ 2081 cb_data.args.hipGetDeviceProperties.deviceId = device; \ 2084 #define INIT_hipFreeArray_CB_ARGS_DATA(cb_data) { \ 2085 cb_data.args.hipFreeArray.array = array; \ 2088 #define INIT_hipEventElapsedTime_CB_ARGS_DATA(cb_data) { \ 2089 cb_data.args.hipEventElapsedTime.ms = ms; \ 2090 cb_data.args.hipEventElapsedTime.start = start; \ 2091 cb_data.args.hipEventElapsedTime.stop = stop; \ 2094 #define INIT_hipDevicePrimaryCtxRelease_CB_ARGS_DATA(cb_data) { \ 2095 cb_data.args.hipDevicePrimaryCtxRelease.dev = dev; \ 2098 #define INIT_hipHostGetDevicePointer_CB_ARGS_DATA(cb_data) { \ 2099 cb_data.args.hipHostGetDevicePointer.devPtr = devicePointer; \ 2100 cb_data.args.hipHostGetDevicePointer.hstPtr = hostPointer; \ 2101 cb_data.args.hipHostGetDevicePointer.flags = flags; \ 2104 #define INIT_hipMemcpyParam2D_CB_ARGS_DATA(cb_data) { \ 2105 cb_data.args.hipMemcpyParam2D.pCopy = pCopy; \ 2108 #define INIT_hipModuleGetFunction_CB_ARGS_DATA(cb_data) { \ 2109 cb_data.args.hipModuleGetFunction.function = hfunc; \ 2110 cb_data.args.hipModuleGetFunction.module = hmod; \ 2111 cb_data.args.hipModuleGetFunction.kname = name; \ 2114 #define INIT_hipMemsetD32Async_CB_ARGS_DATA(cb_data) { \ 2115 cb_data.args.hipMemsetD32Async.dst = dst; \ 2116 cb_data.args.hipMemsetD32Async.value = value; \ 2117 cb_data.args.hipMemsetD32Async.count = count; \ 2118 cb_data.args.hipMemsetD32Async.stream = stream; \ 2121 #define INIT_hipGetDevice_CB_ARGS_DATA(cb_data) { \ 2122 cb_data.args.hipGetDevice.deviceId = deviceId; \ 2125 #define INIT_hipGetDeviceCount_CB_ARGS_DATA(cb_data) { \ 2126 cb_data.args.hipGetDeviceCount.count = count; \ 2128 #define INIT_CB_ARGS_DATA(cb_id, cb_data) INIT_##cb_id##_CB_ARGS_DATA(cb_data) 2129 #endif // _HIP_PROF_STR_H Definition: hip_runtime_api.h:283
Definition: driver_types.h:241
Definition: hip_runtime_api.h:151
Definition: hip_module.cpp:108
Definition: hip_runtime_api.h:121
Definition: hip_hcc_internal.h:910
Definition: texture_types.h:74
Definition: driver_types.h:78
hipDeviceAttribute_t
Definition: hip_runtime_api.h:279
Definition: hip_runtime_api.h:274
void(* hipStreamCallback_t)(hipStream_t stream, hipError_t status, void *userData)
Definition: hip_runtime_api.h:848
Definition: driver_types.h:69
Definition: driver_types.h:254
Definition: driver_types.h:62
Definition: driver_types.h:234
hipFuncCache_t
Definition: hip_runtime_api.h:250
Definition: hip_runtime_api.h:83
hipSharedMemConfig
Definition: hip_runtime_api.h:261
Definition: hip_hcc_internal.h:732
Definition: hip_hcc_internal.h:556
Definition: driver_types.h:91
Definition: hip_runtime_api.h:106
Definition: hip_hcc_internal.h:405
Definition: hip_prof_str.h:411