2 #ifndef _HIP_PROF_STR_H 3 #define _HIP_PROF_STR_H 8 #define INIT_NONE_CB_ARGS_DATA(cb_data) {}; 9 #define INIT_hipGetTextureAlignmentOffset_CB_ARGS_DATA(cb_data) {}; 10 #define INIT_hipDestroyTextureObject_CB_ARGS_DATA(cb_data) {}; 11 #define INIT_hipTexRefSetAddress_CB_ARGS_DATA(cb_data) {}; 12 #define INIT_hipGetTextureObjectTextureDesc_CB_ARGS_DATA(cb_data) {}; 13 #define INIT_hipBindTexture2D_CB_ARGS_DATA(cb_data) {}; 14 #define INIT_hipTexRefSetAddressMode_CB_ARGS_DATA(cb_data) {}; 15 #define INIT_hipCreateTextureObject_CB_ARGS_DATA(cb_data) {}; 16 #define INIT_hipBindTextureToMipmappedArray_CB_ARGS_DATA(cb_data) {}; 17 #define INIT_hipBindTextureToArray_CB_ARGS_DATA(cb_data) {}; 18 #define INIT_hipTexRefSetFormat_CB_ARGS_DATA(cb_data) {}; 19 #define INIT_hipMemcpyHtoH_CB_ARGS_DATA(cb_data) {}; 20 #define INIT_hipTexRefSetArray_CB_ARGS_DATA(cb_data) {}; 21 #define INIT_hipTexRefSetAddress2D_CB_ARGS_DATA(cb_data) {}; 22 #define INIT_hipGetTextureObjectResourceViewDesc_CB_ARGS_DATA(cb_data) {}; 23 #define INIT_hipUnbindTexture_CB_ARGS_DATA(cb_data) {}; 24 #define INIT_hipTexRefSetFilterMode_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_hipHccGetAcceleratorView_CB_ARGS_DATA(cb_data) {}; 28 #define INIT_hipExtModuleLaunchKernel_CB_ARGS_DATA(cb_data) {}; 29 #define INIT_hipGetTextureObjectResourceDesc_CB_ARGS_DATA(cb_data) {}; 30 #define INIT_hipDestroySurfaceObject_CB_ARGS_DATA(cb_data) {}; 31 #define INIT_hipGetTextureReference_CB_ARGS_DATA(cb_data) {}; 32 #define INIT_hipTexRefSetFlags_CB_ARGS_DATA(cb_data) {}; 33 #define INIT_hipBindTexture_CB_ARGS_DATA(cb_data) {}; 34 #define INIT_hipHccGetAccelerator_CB_ARGS_DATA(cb_data) {}; 38 HIP_API_ID_hipStreamCreateWithPriority = 0,
39 HIP_API_ID_hipMemcpyToSymbolAsync = 1,
40 HIP_API_ID_hipMallocPitch = 2,
41 HIP_API_ID_hipMalloc = 3,
42 HIP_API_ID_hipDeviceGetName = 4,
43 HIP_API_ID_hipEventRecord = 5,
44 HIP_API_ID_hipCtxSynchronize = 6,
45 HIP_API_ID_hipSetDevice = 7,
46 HIP_API_ID_hipCtxGetApiVersion = 8,
47 HIP_API_ID_hipSetupArgument = 9,
48 HIP_API_ID_hipMemcpyFromSymbolAsync = 10,
49 HIP_API_ID_hipMemcpyDtoD = 11,
50 HIP_API_ID_hipHostFree = 12,
51 HIP_API_ID_hipMemcpy2DToArray = 13,
52 HIP_API_ID_hipCtxGetCacheConfig = 14,
53 HIP_API_ID_hipStreamWaitEvent = 15,
54 HIP_API_ID_hipDeviceGetStreamPriorityRange = 16,
55 HIP_API_ID_hipModuleLoad = 17,
56 HIP_API_ID_hipDevicePrimaryCtxSetFlags = 18,
57 HIP_API_ID_hipMemcpyAsync = 19,
58 HIP_API_ID_hipMalloc3DArray = 20,
59 HIP_API_ID_hipStreamCreate = 21,
60 HIP_API_ID_hipCtxGetCurrent = 22,
61 HIP_API_ID_hipDevicePrimaryCtxGetState = 23,
62 HIP_API_ID_hipEventQuery = 24,
63 HIP_API_ID_hipEventCreate = 25,
64 HIP_API_ID_hipMemGetAddressRange = 26,
65 HIP_API_ID_hipMemcpyFromSymbol = 27,
66 HIP_API_ID_hipArrayCreate = 28,
67 HIP_API_ID_hipStreamGetFlags = 29,
68 HIP_API_ID_hipMallocArray = 30,
69 HIP_API_ID_hipCtxGetSharedMemConfig = 31,
70 HIP_API_ID_hipMemPtrGetInfo = 32,
71 HIP_API_ID_hipCtxGetFlags = 33,
72 HIP_API_ID_hipStreamDestroy = 34,
73 HIP_API_ID_hipMemset3DAsync = 35,
74 HIP_API_ID_hipMemcpy3D = 36,
75 HIP_API_ID_hipInit = 37,
76 HIP_API_ID_hipMemcpyAtoH = 38,
77 HIP_API_ID_hipStreamGetPriority = 39,
78 HIP_API_ID_hipMemset2D = 40,
79 HIP_API_ID_hipMemset2DAsync = 41,
80 HIP_API_ID_hipDeviceCanAccessPeer = 42,
81 HIP_API_ID_hipDeviceEnablePeerAccess = 43,
82 HIP_API_ID_hipModuleUnload = 44,
83 HIP_API_ID_hipHostUnregister = 45,
84 HIP_API_ID_hipProfilerStop = 46,
85 HIP_API_ID_hipLaunchByPtr = 47,
86 HIP_API_ID_hipStreamSynchronize = 48,
87 HIP_API_ID_hipDeviceSetCacheConfig = 49,
88 HIP_API_ID_hipGetErrorName = 50,
89 HIP_API_ID_hipMemcpyHtoD = 51,
90 HIP_API_ID_hipModuleGetGlobal = 52,
91 HIP_API_ID_hipMemcpyHtoA = 53,
92 HIP_API_ID_hipCtxCreate = 54,
93 HIP_API_ID_hipMemcpy2D = 55,
94 HIP_API_ID_hipIpcCloseMemHandle = 56,
95 HIP_API_ID_hipChooseDevice = 57,
96 HIP_API_ID_hipDeviceSetSharedMemConfig = 58,
97 HIP_API_ID_hipDeviceComputeCapability = 59,
98 HIP_API_ID_hipDeviceGet = 60,
99 HIP_API_ID_hipProfilerStart = 61,
100 HIP_API_ID_hipCtxSetCacheConfig = 62,
101 HIP_API_ID_hipFuncSetCacheConfig = 63,
102 HIP_API_ID_hipMemcpyPeerAsync = 64,
103 HIP_API_ID_hipEventElapsedTime = 65,
104 HIP_API_ID_hipDevicePrimaryCtxReset = 66,
105 HIP_API_ID_hipEventDestroy = 67,
106 HIP_API_ID_hipCtxPopCurrent = 68,
107 HIP_API_ID_hipGetSymbolAddress = 69,
108 HIP_API_ID_hipHostGetFlags = 70,
109 HIP_API_ID_hipHostMalloc = 71,
110 HIP_API_ID_hipDriverGetVersion = 72,
111 HIP_API_ID_hipMemGetInfo = 73,
112 HIP_API_ID_hipDeviceReset = 74,
113 HIP_API_ID_hipMemset = 75,
114 HIP_API_ID_hipMemsetD8 = 76,
115 HIP_API_ID_hipHostRegister = 77,
116 HIP_API_ID_hipCtxSetSharedMemConfig = 78,
117 HIP_API_ID_hipArray3DCreate = 79,
118 HIP_API_ID_hipIpcOpenMemHandle = 80,
119 HIP_API_ID_hipGetLastError = 81,
120 HIP_API_ID_hipCtxDestroy = 82,
121 HIP_API_ID_hipDeviceGetSharedMemConfig = 83,
122 HIP_API_ID_hipSetDeviceFlags = 84,
123 HIP_API_ID_hipHccModuleLaunchKernel = 85,
124 HIP_API_ID_hipFree = 86,
125 HIP_API_ID_hipDeviceGetAttribute = 87,
126 HIP_API_ID_hipMemcpyDtoH = 88,
127 HIP_API_ID_hipCtxDisablePeerAccess = 89,
128 HIP_API_ID_hipDeviceGetByPCIBusId = 90,
129 HIP_API_ID_hipIpcGetMemHandle = 91,
130 HIP_API_ID_hipMemcpyHtoDAsync = 92,
131 HIP_API_ID_hipCtxGetDevice = 93,
132 HIP_API_ID_hipMemset3D = 94,
133 HIP_API_ID_hipModuleLoadData = 95,
134 HIP_API_ID_hipDeviceTotalMem = 96,
135 HIP_API_ID_hipCtxSetCurrent = 97,
136 HIP_API_ID_hipGetErrorString = 98,
137 HIP_API_ID_hipDevicePrimaryCtxRetain = 99,
138 HIP_API_ID_hipDeviceDisablePeerAccess = 100,
139 HIP_API_ID_hipStreamCreateWithFlags = 101,
140 HIP_API_ID_hipMemcpyFromArray = 102,
141 HIP_API_ID_hipMemcpy2DAsync = 103,
142 HIP_API_ID_hipGetSymbolSize = 104,
143 HIP_API_ID_hipEventCreateWithFlags = 105,
144 HIP_API_ID_hipStreamQuery = 106,
145 HIP_API_ID_hipDeviceGetPCIBusId = 107,
146 HIP_API_ID_hipMemcpy = 108,
147 HIP_API_ID_hipPeekAtLastError = 109,
148 HIP_API_ID_hipStreamAddCallback = 110,
149 HIP_API_ID_hipMemcpyToArray = 111,
150 HIP_API_ID_hipMemsetD32 = 112,
151 HIP_API_ID_hipDeviceSynchronize = 113,
152 HIP_API_ID_hipDeviceGetCacheConfig = 114,
153 HIP_API_ID_hipMalloc3D = 115,
154 HIP_API_ID_hipPointerGetAttributes = 116,
155 HIP_API_ID_hipMemsetAsync = 117,
156 HIP_API_ID_hipMemcpyToSymbol = 118,
157 HIP_API_ID_hipCtxPushCurrent = 119,
158 HIP_API_ID_hipMemcpyPeer = 120,
159 HIP_API_ID_hipEventSynchronize = 121,
160 HIP_API_ID_hipMemcpyDtoDAsync = 122,
161 HIP_API_ID_hipExtMallocWithFlags = 123,
162 HIP_API_ID_hipCtxEnablePeerAccess = 124,
163 HIP_API_ID_hipMemcpyDtoHAsync = 125,
164 HIP_API_ID_hipModuleLaunchKernel = 126,
165 HIP_API_ID_hipModuleGetTexRef = 127,
166 HIP_API_ID_hipDeviceGetLimit = 128,
167 HIP_API_ID_hipModuleLoadDataEx = 129,
168 HIP_API_ID_hipRuntimeGetVersion = 130,
169 HIP_API_ID_hipGetDeviceProperties = 131,
170 HIP_API_ID_hipFreeArray = 132,
171 HIP_API_ID_hipDevicePrimaryCtxRelease = 133,
172 HIP_API_ID_hipHostGetDevicePointer = 134,
173 HIP_API_ID_hipMemcpyParam2D = 135,
174 HIP_API_ID_hipModuleGetFunction = 136,
175 HIP_API_ID_hipMemsetD32Async = 137,
176 HIP_API_ID_hipGetDevice = 138,
177 HIP_API_ID_hipGetDeviceCount = 139,
178 HIP_API_ID_NUMBER = 140,
179 HIP_API_ID_ANY = 141,
181 HIP_API_ID_NONE = HIP_API_ID_NUMBER,
182 HIP_API_ID_hipGetTextureAlignmentOffset = HIP_API_ID_NUMBER,
183 HIP_API_ID_hipDestroyTextureObject = HIP_API_ID_NUMBER,
184 HIP_API_ID_hipTexRefSetAddress = HIP_API_ID_NUMBER,
185 HIP_API_ID_hipGetTextureObjectTextureDesc = HIP_API_ID_NUMBER,
186 HIP_API_ID_hipBindTexture2D = HIP_API_ID_NUMBER,
187 HIP_API_ID_hipTexRefSetAddressMode = HIP_API_ID_NUMBER,
188 HIP_API_ID_hipCreateTextureObject = HIP_API_ID_NUMBER,
189 HIP_API_ID_hipBindTextureToMipmappedArray = HIP_API_ID_NUMBER,
190 HIP_API_ID_hipBindTextureToArray = HIP_API_ID_NUMBER,
191 HIP_API_ID_hipTexRefSetFormat = HIP_API_ID_NUMBER,
192 HIP_API_ID_hipMemcpyHtoH = HIP_API_ID_NUMBER,
193 HIP_API_ID_hipTexRefSetArray = HIP_API_ID_NUMBER,
194 HIP_API_ID_hipTexRefSetAddress2D = HIP_API_ID_NUMBER,
195 HIP_API_ID_hipGetTextureObjectResourceViewDesc = HIP_API_ID_NUMBER,
196 HIP_API_ID_hipUnbindTexture = HIP_API_ID_NUMBER,
197 HIP_API_ID_hipTexRefSetFilterMode = HIP_API_ID_NUMBER,
198 HIP_API_ID_hipCreateSurfaceObject = HIP_API_ID_NUMBER,
199 HIP_API_ID_hipGetChannelDesc = HIP_API_ID_NUMBER,
200 HIP_API_ID_hipHccGetAcceleratorView = HIP_API_ID_NUMBER,
201 HIP_API_ID_hipExtModuleLaunchKernel = HIP_API_ID_NUMBER,
202 HIP_API_ID_hipGetTextureObjectResourceDesc = HIP_API_ID_NUMBER,
203 HIP_API_ID_hipDestroySurfaceObject = HIP_API_ID_NUMBER,
204 HIP_API_ID_hipGetTextureReference = HIP_API_ID_NUMBER,
205 HIP_API_ID_hipTexRefSetFlags = HIP_API_ID_NUMBER,
206 HIP_API_ID_hipBindTexture = HIP_API_ID_NUMBER,
207 HIP_API_ID_hipHccGetAccelerator = HIP_API_ID_NUMBER,
211 static const char* hip_api_name(
const uint32_t&
id) {
213 case HIP_API_ID_hipStreamCreateWithPriority:
return "hipStreamCreateWithPriority";
214 case HIP_API_ID_hipMemcpyToSymbolAsync:
return "hipMemcpyToSymbolAsync";
215 case HIP_API_ID_hipMallocPitch:
return "hipMallocPitch";
216 case HIP_API_ID_hipMalloc:
return "hipMalloc";
217 case HIP_API_ID_hipDeviceGetName:
return "hipDeviceGetName";
218 case HIP_API_ID_hipEventRecord:
return "hipEventRecord";
219 case HIP_API_ID_hipCtxSynchronize:
return "hipCtxSynchronize";
220 case HIP_API_ID_hipSetDevice:
return "hipSetDevice";
221 case HIP_API_ID_hipCtxGetApiVersion:
return "hipCtxGetApiVersion";
222 case HIP_API_ID_hipSetupArgument:
return "hipSetupArgument";
223 case HIP_API_ID_hipMemcpyFromSymbolAsync:
return "hipMemcpyFromSymbolAsync";
224 case HIP_API_ID_hipMemcpyDtoD:
return "hipMemcpyDtoD";
225 case HIP_API_ID_hipHostFree:
return "hipHostFree";
226 case HIP_API_ID_hipMemcpy2DToArray:
return "hipMemcpy2DToArray";
227 case HIP_API_ID_hipCtxGetCacheConfig:
return "hipCtxGetCacheConfig";
228 case HIP_API_ID_hipStreamWaitEvent:
return "hipStreamWaitEvent";
229 case HIP_API_ID_hipDeviceGetStreamPriorityRange:
return "hipDeviceGetStreamPriorityRange";
230 case HIP_API_ID_hipModuleLoad:
return "hipModuleLoad";
231 case HIP_API_ID_hipDevicePrimaryCtxSetFlags:
return "hipDevicePrimaryCtxSetFlags";
232 case HIP_API_ID_hipMemcpyAsync:
return "hipMemcpyAsync";
233 case HIP_API_ID_hipMalloc3DArray:
return "hipMalloc3DArray";
234 case HIP_API_ID_hipStreamCreate:
return "hipStreamCreate";
235 case HIP_API_ID_hipCtxGetCurrent:
return "hipCtxGetCurrent";
236 case HIP_API_ID_hipDevicePrimaryCtxGetState:
return "hipDevicePrimaryCtxGetState";
237 case HIP_API_ID_hipEventQuery:
return "hipEventQuery";
238 case HIP_API_ID_hipEventCreate:
return "hipEventCreate";
239 case HIP_API_ID_hipMemGetAddressRange:
return "hipMemGetAddressRange";
240 case HIP_API_ID_hipMemcpyFromSymbol:
return "hipMemcpyFromSymbol";
241 case HIP_API_ID_hipArrayCreate:
return "hipArrayCreate";
242 case HIP_API_ID_hipStreamGetFlags:
return "hipStreamGetFlags";
243 case HIP_API_ID_hipMallocArray:
return "hipMallocArray";
244 case HIP_API_ID_hipCtxGetSharedMemConfig:
return "hipCtxGetSharedMemConfig";
245 case HIP_API_ID_hipMemPtrGetInfo:
return "hipMemPtrGetInfo";
246 case HIP_API_ID_hipCtxGetFlags:
return "hipCtxGetFlags";
247 case HIP_API_ID_hipStreamDestroy:
return "hipStreamDestroy";
248 case HIP_API_ID_hipMemset3DAsync:
return "hipMemset3DAsync";
249 case HIP_API_ID_hipMemcpy3D:
return "hipMemcpy3D";
250 case HIP_API_ID_hipInit:
return "hipInit";
251 case HIP_API_ID_hipMemcpyAtoH:
return "hipMemcpyAtoH";
252 case HIP_API_ID_hipStreamGetPriority:
return "hipStreamGetPriority";
253 case HIP_API_ID_hipMemset2D:
return "hipMemset2D";
254 case HIP_API_ID_hipMemset2DAsync:
return "hipMemset2DAsync";
255 case HIP_API_ID_hipDeviceCanAccessPeer:
return "hipDeviceCanAccessPeer";
256 case HIP_API_ID_hipDeviceEnablePeerAccess:
return "hipDeviceEnablePeerAccess";
257 case HIP_API_ID_hipModuleUnload:
return "hipModuleUnload";
258 case HIP_API_ID_hipHostUnregister:
return "hipHostUnregister";
259 case HIP_API_ID_hipProfilerStop:
return "hipProfilerStop";
260 case HIP_API_ID_hipLaunchByPtr:
return "hipLaunchByPtr";
261 case HIP_API_ID_hipStreamSynchronize:
return "hipStreamSynchronize";
262 case HIP_API_ID_hipDeviceSetCacheConfig:
return "hipDeviceSetCacheConfig";
263 case HIP_API_ID_hipGetErrorName:
return "hipGetErrorName";
264 case HIP_API_ID_hipMemcpyHtoD:
return "hipMemcpyHtoD";
265 case HIP_API_ID_hipModuleGetGlobal:
return "hipModuleGetGlobal";
266 case HIP_API_ID_hipMemcpyHtoA:
return "hipMemcpyHtoA";
267 case HIP_API_ID_hipCtxCreate:
return "hipCtxCreate";
268 case HIP_API_ID_hipMemcpy2D:
return "hipMemcpy2D";
269 case HIP_API_ID_hipIpcCloseMemHandle:
return "hipIpcCloseMemHandle";
270 case HIP_API_ID_hipChooseDevice:
return "hipChooseDevice";
271 case HIP_API_ID_hipDeviceSetSharedMemConfig:
return "hipDeviceSetSharedMemConfig";
272 case HIP_API_ID_hipDeviceComputeCapability:
return "hipDeviceComputeCapability";
273 case HIP_API_ID_hipDeviceGet:
return "hipDeviceGet";
274 case HIP_API_ID_hipProfilerStart:
return "hipProfilerStart";
275 case HIP_API_ID_hipCtxSetCacheConfig:
return "hipCtxSetCacheConfig";
276 case HIP_API_ID_hipFuncSetCacheConfig:
return "hipFuncSetCacheConfig";
277 case HIP_API_ID_hipMemcpyPeerAsync:
return "hipMemcpyPeerAsync";
278 case HIP_API_ID_hipEventElapsedTime:
return "hipEventElapsedTime";
279 case HIP_API_ID_hipDevicePrimaryCtxReset:
return "hipDevicePrimaryCtxReset";
280 case HIP_API_ID_hipEventDestroy:
return "hipEventDestroy";
281 case HIP_API_ID_hipCtxPopCurrent:
return "hipCtxPopCurrent";
282 case HIP_API_ID_hipGetSymbolAddress:
return "hipGetSymbolAddress";
283 case HIP_API_ID_hipHostGetFlags:
return "hipHostGetFlags";
284 case HIP_API_ID_hipHostMalloc:
return "hipHostMalloc";
285 case HIP_API_ID_hipDriverGetVersion:
return "hipDriverGetVersion";
286 case HIP_API_ID_hipMemGetInfo:
return "hipMemGetInfo";
287 case HIP_API_ID_hipDeviceReset:
return "hipDeviceReset";
288 case HIP_API_ID_hipMemset:
return "hipMemset";
289 case HIP_API_ID_hipMemsetD8:
return "hipMemsetD8";
290 case HIP_API_ID_hipHostRegister:
return "hipHostRegister";
291 case HIP_API_ID_hipCtxSetSharedMemConfig:
return "hipCtxSetSharedMemConfig";
292 case HIP_API_ID_hipArray3DCreate:
return "hipArray3DCreate";
293 case HIP_API_ID_hipIpcOpenMemHandle:
return "hipIpcOpenMemHandle";
294 case HIP_API_ID_hipGetLastError:
return "hipGetLastError";
295 case HIP_API_ID_hipCtxDestroy:
return "hipCtxDestroy";
296 case HIP_API_ID_hipDeviceGetSharedMemConfig:
return "hipDeviceGetSharedMemConfig";
297 case HIP_API_ID_hipSetDeviceFlags:
return "hipSetDeviceFlags";
298 case HIP_API_ID_hipHccModuleLaunchKernel:
return "hipHccModuleLaunchKernel";
299 case HIP_API_ID_hipFree:
return "hipFree";
300 case HIP_API_ID_hipDeviceGetAttribute:
return "hipDeviceGetAttribute";
301 case HIP_API_ID_hipMemcpyDtoH:
return "hipMemcpyDtoH";
302 case HIP_API_ID_hipCtxDisablePeerAccess:
return "hipCtxDisablePeerAccess";
303 case HIP_API_ID_hipDeviceGetByPCIBusId:
return "hipDeviceGetByPCIBusId";
304 case HIP_API_ID_hipIpcGetMemHandle:
return "hipIpcGetMemHandle";
305 case HIP_API_ID_hipMemcpyHtoDAsync:
return "hipMemcpyHtoDAsync";
306 case HIP_API_ID_hipCtxGetDevice:
return "hipCtxGetDevice";
307 case HIP_API_ID_hipMemset3D:
return "hipMemset3D";
308 case HIP_API_ID_hipModuleLoadData:
return "hipModuleLoadData";
309 case HIP_API_ID_hipDeviceTotalMem:
return "hipDeviceTotalMem";
310 case HIP_API_ID_hipCtxSetCurrent:
return "hipCtxSetCurrent";
311 case HIP_API_ID_hipGetErrorString:
return "hipGetErrorString";
312 case HIP_API_ID_hipDevicePrimaryCtxRetain:
return "hipDevicePrimaryCtxRetain";
313 case HIP_API_ID_hipDeviceDisablePeerAccess:
return "hipDeviceDisablePeerAccess";
314 case HIP_API_ID_hipStreamCreateWithFlags:
return "hipStreamCreateWithFlags";
315 case HIP_API_ID_hipMemcpyFromArray:
return "hipMemcpyFromArray";
316 case HIP_API_ID_hipMemcpy2DAsync:
return "hipMemcpy2DAsync";
317 case HIP_API_ID_hipGetSymbolSize:
return "hipGetSymbolSize";
318 case HIP_API_ID_hipEventCreateWithFlags:
return "hipEventCreateWithFlags";
319 case HIP_API_ID_hipStreamQuery:
return "hipStreamQuery";
320 case HIP_API_ID_hipDeviceGetPCIBusId:
return "hipDeviceGetPCIBusId";
321 case HIP_API_ID_hipMemcpy:
return "hipMemcpy";
322 case HIP_API_ID_hipPeekAtLastError:
return "hipPeekAtLastError";
323 case HIP_API_ID_hipStreamAddCallback:
return "hipStreamAddCallback";
324 case HIP_API_ID_hipMemcpyToArray:
return "hipMemcpyToArray";
325 case HIP_API_ID_hipMemsetD32:
return "hipMemsetD32";
326 case HIP_API_ID_hipDeviceSynchronize:
return "hipDeviceSynchronize";
327 case HIP_API_ID_hipDeviceGetCacheConfig:
return "hipDeviceGetCacheConfig";
328 case HIP_API_ID_hipMalloc3D:
return "hipMalloc3D";
329 case HIP_API_ID_hipPointerGetAttributes:
return "hipPointerGetAttributes";
330 case HIP_API_ID_hipMemsetAsync:
return "hipMemsetAsync";
331 case HIP_API_ID_hipMemcpyToSymbol:
return "hipMemcpyToSymbol";
332 case HIP_API_ID_hipCtxPushCurrent:
return "hipCtxPushCurrent";
333 case HIP_API_ID_hipMemcpyPeer:
return "hipMemcpyPeer";
334 case HIP_API_ID_hipEventSynchronize:
return "hipEventSynchronize";
335 case HIP_API_ID_hipMemcpyDtoDAsync:
return "hipMemcpyDtoDAsync";
336 case HIP_API_ID_hipExtMallocWithFlags:
return "hipExtMallocWithFlags";
337 case HIP_API_ID_hipCtxEnablePeerAccess:
return "hipCtxEnablePeerAccess";
338 case HIP_API_ID_hipMemcpyDtoHAsync:
return "hipMemcpyDtoHAsync";
339 case HIP_API_ID_hipModuleLaunchKernel:
return "hipModuleLaunchKernel";
340 case HIP_API_ID_hipModuleGetTexRef:
return "hipModuleGetTexRef";
341 case HIP_API_ID_hipDeviceGetLimit:
return "hipDeviceGetLimit";
342 case HIP_API_ID_hipModuleLoadDataEx:
return "hipModuleLoadDataEx";
343 case HIP_API_ID_hipRuntimeGetVersion:
return "hipRuntimeGetVersion";
344 case HIP_API_ID_hipGetDeviceProperties:
return "hipGetDeviceProperties";
345 case HIP_API_ID_hipFreeArray:
return "hipFreeArray";
346 case HIP_API_ID_hipDevicePrimaryCtxRelease:
return "hipDevicePrimaryCtxRelease";
347 case HIP_API_ID_hipHostGetDevicePointer:
return "hipHostGetDevicePointer";
348 case HIP_API_ID_hipMemcpyParam2D:
return "hipMemcpyParam2D";
349 case HIP_API_ID_hipModuleGetFunction:
return "hipModuleGetFunction";
350 case HIP_API_ID_hipMemsetD32Async:
return "hipMemsetD32Async";
351 case HIP_API_ID_hipGetDevice:
return "hipGetDevice";
352 case HIP_API_ID_hipGetDeviceCount:
return "hipGetDeviceCount";
359 uint64_t correlation_id;
366 } hipStreamCreateWithPriority;
368 const void* symbolName;
374 } hipMemcpyToSymbolAsync;
400 } hipCtxGetApiVersion;
408 const void* symbolName;
413 } hipMemcpyFromSymbolAsync;
431 } hipMemcpy2DToArray;
434 } hipCtxGetCacheConfig;
439 } hipStreamWaitEvent;
442 int* greatestPriority;
443 } hipDeviceGetStreamPriorityRange;
451 } hipDevicePrimaryCtxSetFlags;
475 } hipDevicePrimaryCtxGetState;
483 hipDeviceptr_t* pbase;
486 } hipMemGetAddressRange;
489 const void* symbolName;
493 } hipMemcpyFromSymbol;
511 } hipCtxGetSharedMemConfig;
543 } hipStreamGetPriority;
563 } hipDeviceCanAccessPeer;
567 } hipDeviceEnablePeerAccess;
579 } hipStreamSynchronize;
582 } hipDeviceSetCacheConfig;
584 hipError_t hip_error;
592 hipDeviceptr_t* dptr;
596 } hipModuleGetGlobal;
619 } hipIpcCloseMemHandle;
626 } hipDeviceSetSharedMemConfig;
631 } hipDeviceComputeCapability;
638 } hipCtxSetCacheConfig;
642 } hipFuncSetCacheConfig;
650 } hipMemcpyPeerAsync;
655 } hipEventElapsedTime;
658 } hipDevicePrimaryCtxReset;
667 const void* symbolName;
668 } hipGetSymbolAddress;
670 unsigned int* flagsPtr;
680 } hipDriverGetVersion;
702 } hipCtxSetSharedMemConfig;
711 } hipIpcOpenMemHandle;
717 } hipDeviceGetSharedMemConfig;
723 unsigned int globalWorkSizeX;
724 unsigned int globalWorkSizeY;
725 unsigned int globalWorkSizeZ;
726 unsigned int localWorkSizeX;
727 unsigned int localWorkSizeY;
728 unsigned int localWorkSizeZ;
729 size_t sharedMemBytes;
735 } hipHccModuleLaunchKernel;
743 } hipDeviceGetAttribute;
751 } hipCtxDisablePeerAccess;
754 const char* pciBusId;
755 } hipDeviceGetByPCIBusId;
759 } hipIpcGetMemHandle;
765 } hipMemcpyHtoDAsync;
791 } hipDevicePrimaryCtxRetain;
794 } hipDeviceDisablePeerAccess;
798 } hipStreamCreateWithFlags;
806 } hipMemcpyFromArray;
819 const void* symbolName;
824 } hipEventCreateWithFlags;
832 } hipDeviceGetPCIBusId;
844 } hipStreamAddCallback;
860 } hipDeviceGetCacheConfig;
868 } hipPointerGetAttributes;
876 const void* symbolName;
894 } hipEventSynchronize;
900 } hipMemcpyDtoDAsync;
905 } hipExtMallocWithFlags;
909 } hipCtxEnablePeerAccess;
915 } hipMemcpyDtoHAsync;
918 unsigned int gridDimX;
919 unsigned int gridDimY;
920 unsigned int gridDimZ;
921 unsigned int blockDimX;
922 unsigned int blockDimY;
923 unsigned int blockDimZ;
924 unsigned int sharedMemBytes;
928 } hipModuleLaunchKernel;
933 } hipModuleGetTexRef;
941 unsigned int numOptions;
942 hipJitOption* options;
944 } hipModuleLoadDataEx;
947 } hipRuntimeGetVersion;
951 } hipGetDeviceProperties;
957 } hipDevicePrimaryCtxRelease;
962 } hipHostGetDevicePointer;
970 } hipModuleGetFunction;
988 #define INIT_hipStreamCreateWithPriority_CB_ARGS_DATA(cb_data) { \ 989 cb_data.args.hipStreamCreateWithPriority.stream = stream; \ 990 cb_data.args.hipStreamCreateWithPriority.flags = flags; \ 991 cb_data.args.hipStreamCreateWithPriority.priority = priority; \ 994 #define INIT_hipMemcpyToSymbolAsync_CB_ARGS_DATA(cb_data) { \ 997 #define INIT_hipMallocPitch_CB_ARGS_DATA(cb_data) { \ 998 cb_data.args.hipMallocPitch.ptr = ptr; \ 999 cb_data.args.hipMallocPitch.pitch = pitch; \ 1000 cb_data.args.hipMallocPitch.width = width; \ 1001 cb_data.args.hipMallocPitch.height = height; \ 1004 #define INIT_hipMalloc_CB_ARGS_DATA(cb_data) { \ 1005 cb_data.args.hipMalloc.ptr = ptr; \ 1006 cb_data.args.hipMalloc.size = sizeBytes; \ 1009 #define INIT_hipDeviceGetName_CB_ARGS_DATA(cb_data) { \ 1010 cb_data.args.hipDeviceGetName.name = name; \ 1011 cb_data.args.hipDeviceGetName.len = len; \ 1012 cb_data.args.hipDeviceGetName.device = device; \ 1015 #define INIT_hipEventRecord_CB_ARGS_DATA(cb_data) { \ 1016 cb_data.args.hipEventRecord.event = event; \ 1017 cb_data.args.hipEventRecord.stream = stream; \ 1020 #define INIT_hipCtxSynchronize_CB_ARGS_DATA(cb_data) { \ 1023 #define INIT_hipSetDevice_CB_ARGS_DATA(cb_data) { \ 1024 cb_data.args.hipSetDevice.deviceId = deviceId; \ 1027 #define INIT_hipCtxGetApiVersion_CB_ARGS_DATA(cb_data) { \ 1028 cb_data.args.hipCtxGetApiVersion.ctx = ctx; \ 1029 cb_data.args.hipCtxGetApiVersion.apiVersion = apiVersion; \ 1032 #define INIT_hipSetupArgument_CB_ARGS_DATA(cb_data) { \ 1033 cb_data.args.hipSetupArgument.arg = arg; \ 1034 cb_data.args.hipSetupArgument.size = size; \ 1035 cb_data.args.hipSetupArgument.offset = offset; \ 1038 #define INIT_hipMemcpyFromSymbolAsync_CB_ARGS_DATA(cb_data) { \ 1041 #define INIT_hipMemcpyDtoD_CB_ARGS_DATA(cb_data) { \ 1042 cb_data.args.hipMemcpyDtoD.dst = dst; \ 1043 cb_data.args.hipMemcpyDtoD.src = src; \ 1044 cb_data.args.hipMemcpyDtoD.sizeBytes = sizeBytes; \ 1047 #define INIT_hipHostFree_CB_ARGS_DATA(cb_data) { \ 1048 cb_data.args.hipHostFree.ptr = ptr; \ 1051 #define INIT_hipMemcpy2DToArray_CB_ARGS_DATA(cb_data) { \ 1052 cb_data.args.hipMemcpy2DToArray.dst = dst; \ 1053 cb_data.args.hipMemcpy2DToArray.wOffset = wOffset; \ 1054 cb_data.args.hipMemcpy2DToArray.hOffset = hOffset; \ 1055 cb_data.args.hipMemcpy2DToArray.src = src; \ 1056 cb_data.args.hipMemcpy2DToArray.spitch = spitch; \ 1057 cb_data.args.hipMemcpy2DToArray.width = width; \ 1058 cb_data.args.hipMemcpy2DToArray.height = height; \ 1059 cb_data.args.hipMemcpy2DToArray.kind = kind; \ 1062 #define INIT_hipCtxGetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1063 cb_data.args.hipCtxGetCacheConfig.cacheConfig = cacheConfig; \ 1066 #define INIT_hipStreamWaitEvent_CB_ARGS_DATA(cb_data) { \ 1067 cb_data.args.hipStreamWaitEvent.stream = stream; \ 1068 cb_data.args.hipStreamWaitEvent.event = event; \ 1069 cb_data.args.hipStreamWaitEvent.flags = flags; \ 1072 #define INIT_hipDeviceGetStreamPriorityRange_CB_ARGS_DATA(cb_data) { \ 1073 cb_data.args.hipDeviceGetStreamPriorityRange.leastPriority = leastPriority; \ 1074 cb_data.args.hipDeviceGetStreamPriorityRange.greatestPriority = greatestPriority; \ 1077 #define INIT_hipModuleLoad_CB_ARGS_DATA(cb_data) { \ 1078 cb_data.args.hipModuleLoad.module = module; \ 1079 cb_data.args.hipModuleLoad.fname = fname; \ 1082 #define INIT_hipDevicePrimaryCtxSetFlags_CB_ARGS_DATA(cb_data) { \ 1083 cb_data.args.hipDevicePrimaryCtxSetFlags.dev = dev; \ 1084 cb_data.args.hipDevicePrimaryCtxSetFlags.flags = flags; \ 1087 #define INIT_hipMemcpyAsync_CB_ARGS_DATA(cb_data) { \ 1088 cb_data.args.hipMemcpyAsync.dst = dst; \ 1089 cb_data.args.hipMemcpyAsync.src = src; \ 1090 cb_data.args.hipMemcpyAsync.sizeBytes = sizeBytes; \ 1091 cb_data.args.hipMemcpyAsync.kind = kind; \ 1092 cb_data.args.hipMemcpyAsync.stream = stream; \ 1095 #define INIT_hipMalloc3DArray_CB_ARGS_DATA(cb_data) { \ 1096 cb_data.args.hipMalloc3DArray.array = array; \ 1097 cb_data.args.hipMalloc3DArray.desc = desc; \ 1098 cb_data.args.hipMalloc3DArray.extent = extent; \ 1099 cb_data.args.hipMalloc3DArray.flags = flags; \ 1102 #define INIT_hipStreamCreate_CB_ARGS_DATA(cb_data) { \ 1103 cb_data.args.hipStreamCreate.stream = stream; \ 1106 #define INIT_hipCtxGetCurrent_CB_ARGS_DATA(cb_data) { \ 1107 cb_data.args.hipCtxGetCurrent.ctx = ctx; \ 1110 #define INIT_hipDevicePrimaryCtxGetState_CB_ARGS_DATA(cb_data) { \ 1111 cb_data.args.hipDevicePrimaryCtxGetState.dev = dev; \ 1112 cb_data.args.hipDevicePrimaryCtxGetState.flags = flags; \ 1113 cb_data.args.hipDevicePrimaryCtxGetState.active = active; \ 1116 #define INIT_hipEventQuery_CB_ARGS_DATA(cb_data) { \ 1117 cb_data.args.hipEventQuery.event = event; \ 1120 #define INIT_hipEventCreate_CB_ARGS_DATA(cb_data) { \ 1121 cb_data.args.hipEventCreate.event = event; \ 1124 #define INIT_hipMemGetAddressRange_CB_ARGS_DATA(cb_data) { \ 1125 cb_data.args.hipMemGetAddressRange.pbase = pbase; \ 1126 cb_data.args.hipMemGetAddressRange.psize = psize; \ 1127 cb_data.args.hipMemGetAddressRange.dptr = dptr; \ 1130 #define INIT_hipMemcpyFromSymbol_CB_ARGS_DATA(cb_data) { \ 1133 #define INIT_hipArrayCreate_CB_ARGS_DATA(cb_data) { \ 1134 cb_data.args.hipArrayCreate.pHandle = array; \ 1135 cb_data.args.hipArrayCreate.pAllocateArray = pAllocateArray; \ 1138 #define INIT_hipStreamGetFlags_CB_ARGS_DATA(cb_data) { \ 1139 cb_data.args.hipStreamGetFlags.stream = stream; \ 1140 cb_data.args.hipStreamGetFlags.flags = flags; \ 1143 #define INIT_hipMallocArray_CB_ARGS_DATA(cb_data) { \ 1144 cb_data.args.hipMallocArray.array = array; \ 1145 cb_data.args.hipMallocArray.desc = desc; \ 1146 cb_data.args.hipMallocArray.width = width; \ 1147 cb_data.args.hipMallocArray.height = height; \ 1148 cb_data.args.hipMallocArray.flags = flags; \ 1151 #define INIT_hipCtxGetSharedMemConfig_CB_ARGS_DATA(cb_data) { \ 1152 cb_data.args.hipCtxGetSharedMemConfig.pConfig = pConfig; \ 1155 #define INIT_hipMemPtrGetInfo_CB_ARGS_DATA(cb_data) { \ 1156 cb_data.args.hipMemPtrGetInfo.ptr = ptr; \ 1157 cb_data.args.hipMemPtrGetInfo.size = size; \ 1160 #define INIT_hipCtxGetFlags_CB_ARGS_DATA(cb_data) { \ 1161 cb_data.args.hipCtxGetFlags.flags = flags; \ 1164 #define INIT_hipStreamDestroy_CB_ARGS_DATA(cb_data) { \ 1165 cb_data.args.hipStreamDestroy.stream = stream; \ 1168 #define INIT_hipMemset3DAsync_CB_ARGS_DATA(cb_data) { \ 1169 cb_data.args.hipMemset3DAsync.pitchedDevPtr = pitchedDevPtr; \ 1170 cb_data.args.hipMemset3DAsync.value = value; \ 1171 cb_data.args.hipMemset3DAsync.extent = extent; \ 1172 cb_data.args.hipMemset3DAsync.stream = stream; \ 1175 #define INIT_hipMemcpy3D_CB_ARGS_DATA(cb_data) { \ 1176 cb_data.args.hipMemcpy3D.p = p; \ 1179 #define INIT_hipInit_CB_ARGS_DATA(cb_data) { \ 1180 cb_data.args.hipInit.flags = flags; \ 1183 #define INIT_hipMemcpyAtoH_CB_ARGS_DATA(cb_data) { \ 1184 cb_data.args.hipMemcpyAtoH.dst = dst; \ 1185 cb_data.args.hipMemcpyAtoH.srcArray = srcArray; \ 1186 cb_data.args.hipMemcpyAtoH.srcOffset = srcOffset; \ 1187 cb_data.args.hipMemcpyAtoH.count = count; \ 1190 #define INIT_hipStreamGetPriority_CB_ARGS_DATA(cb_data) { \ 1191 cb_data.args.hipStreamGetPriority.stream = stream; \ 1192 cb_data.args.hipStreamGetPriority.priority = priority; \ 1195 #define INIT_hipMemset2D_CB_ARGS_DATA(cb_data) { \ 1196 cb_data.args.hipMemset2D.dst = dst; \ 1197 cb_data.args.hipMemset2D.pitch = pitch; \ 1198 cb_data.args.hipMemset2D.value = value; \ 1199 cb_data.args.hipMemset2D.width = width; \ 1200 cb_data.args.hipMemset2D.height = height; \ 1203 #define INIT_hipMemset2DAsync_CB_ARGS_DATA(cb_data) { \ 1204 cb_data.args.hipMemset2DAsync.dst = dst; \ 1205 cb_data.args.hipMemset2DAsync.pitch = pitch; \ 1206 cb_data.args.hipMemset2DAsync.value = value; \ 1207 cb_data.args.hipMemset2DAsync.width = width; \ 1208 cb_data.args.hipMemset2DAsync.height = height; \ 1209 cb_data.args.hipMemset2DAsync.stream = stream; \ 1212 #define INIT_hipDeviceCanAccessPeer_CB_ARGS_DATA(cb_data) { \ 1213 cb_data.args.hipDeviceCanAccessPeer.canAccessPeer = canAccessPeer; \ 1214 cb_data.args.hipDeviceCanAccessPeer.deviceId = deviceId; \ 1215 cb_data.args.hipDeviceCanAccessPeer.peerDeviceId = peerDeviceId; \ 1218 #define INIT_hipDeviceEnablePeerAccess_CB_ARGS_DATA(cb_data) { \ 1219 cb_data.args.hipDeviceEnablePeerAccess.peerDeviceId = peerDeviceId; \ 1220 cb_data.args.hipDeviceEnablePeerAccess.flags = flags; \ 1223 #define INIT_hipModuleUnload_CB_ARGS_DATA(cb_data) { \ 1224 cb_data.args.hipModuleUnload.module = hmod; \ 1227 #define INIT_hipHostUnregister_CB_ARGS_DATA(cb_data) { \ 1228 cb_data.args.hipHostUnregister.hostPtr = hostPtr; \ 1231 #define INIT_hipProfilerStop_CB_ARGS_DATA(cb_data) { \ 1234 #define INIT_hipLaunchByPtr_CB_ARGS_DATA(cb_data) { \ 1235 cb_data.args.hipLaunchByPtr.func = hostFunction; \ 1238 #define INIT_hipStreamSynchronize_CB_ARGS_DATA(cb_data) { \ 1239 cb_data.args.hipStreamSynchronize.stream = stream; \ 1242 #define INIT_hipDeviceSetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1243 cb_data.args.hipDeviceSetCacheConfig.cacheConfig = cacheConfig; \ 1246 #define INIT_hipGetErrorName_CB_ARGS_DATA(cb_data) { \ 1247 cb_data.args.hipGetErrorName.hip_error = hip_error; \ 1250 #define INIT_hipMemcpyHtoD_CB_ARGS_DATA(cb_data) { \ 1251 cb_data.args.hipMemcpyHtoD.dst = dst; \ 1252 cb_data.args.hipMemcpyHtoD.src = src; \ 1253 cb_data.args.hipMemcpyHtoD.sizeBytes = sizeBytes; \ 1256 #define INIT_hipModuleGetGlobal_CB_ARGS_DATA(cb_data) { \ 1259 #define INIT_hipMemcpyHtoA_CB_ARGS_DATA(cb_data) { \ 1260 cb_data.args.hipMemcpyHtoA.dstArray = dstArray; \ 1261 cb_data.args.hipMemcpyHtoA.dstOffset = dstOffset; \ 1262 cb_data.args.hipMemcpyHtoA.srcHost = srcHost; \ 1263 cb_data.args.hipMemcpyHtoA.count = count; \ 1266 #define INIT_hipCtxCreate_CB_ARGS_DATA(cb_data) { \ 1267 cb_data.args.hipCtxCreate.ctx = ctx; \ 1268 cb_data.args.hipCtxCreate.flags = flags; \ 1269 cb_data.args.hipCtxCreate.device = device; \ 1272 #define INIT_hipMemcpy2D_CB_ARGS_DATA(cb_data) { \ 1273 cb_data.args.hipMemcpy2D.dst = dst; \ 1274 cb_data.args.hipMemcpy2D.dpitch = dpitch; \ 1275 cb_data.args.hipMemcpy2D.src = src; \ 1276 cb_data.args.hipMemcpy2D.spitch = spitch; \ 1277 cb_data.args.hipMemcpy2D.width = width; \ 1278 cb_data.args.hipMemcpy2D.height = height; \ 1279 cb_data.args.hipMemcpy2D.kind = kind; \ 1282 #define INIT_hipIpcCloseMemHandle_CB_ARGS_DATA(cb_data) { \ 1283 cb_data.args.hipIpcCloseMemHandle.devPtr = devPtr; \ 1286 #define INIT_hipChooseDevice_CB_ARGS_DATA(cb_data) { \ 1287 cb_data.args.hipChooseDevice.device = device; \ 1288 cb_data.args.hipChooseDevice.prop = prop; \ 1291 #define INIT_hipDeviceSetSharedMemConfig_CB_ARGS_DATA(cb_data) { \ 1292 cb_data.args.hipDeviceSetSharedMemConfig.config = config; \ 1295 #define INIT_hipDeviceComputeCapability_CB_ARGS_DATA(cb_data) { \ 1296 cb_data.args.hipDeviceComputeCapability.major = major; \ 1297 cb_data.args.hipDeviceComputeCapability.minor = minor; \ 1298 cb_data.args.hipDeviceComputeCapability.device = device; \ 1301 #define INIT_hipDeviceGet_CB_ARGS_DATA(cb_data) { \ 1302 cb_data.args.hipDeviceGet.device = device; \ 1303 cb_data.args.hipDeviceGet.ordinal = deviceId; \ 1306 #define INIT_hipProfilerStart_CB_ARGS_DATA(cb_data) { \ 1309 #define INIT_hipCtxSetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1310 cb_data.args.hipCtxSetCacheConfig.cacheConfig = cacheConfig; \ 1313 #define INIT_hipFuncSetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1314 cb_data.args.hipFuncSetCacheConfig.func = func; \ 1315 cb_data.args.hipFuncSetCacheConfig.config = cacheConfig; \ 1318 #define INIT_hipMemcpyPeerAsync_CB_ARGS_DATA(cb_data) { \ 1319 cb_data.args.hipMemcpyPeerAsync.dst = dst; \ 1320 cb_data.args.hipMemcpyPeerAsync.dstDeviceId = dstDevice; \ 1321 cb_data.args.hipMemcpyPeerAsync.src = src; \ 1322 cb_data.args.hipMemcpyPeerAsync.srcDevice = srcDevice; \ 1323 cb_data.args.hipMemcpyPeerAsync.sizeBytes = sizeBytes; \ 1324 cb_data.args.hipMemcpyPeerAsync.stream = stream; \ 1327 #define INIT_hipEventElapsedTime_CB_ARGS_DATA(cb_data) { \ 1328 cb_data.args.hipEventElapsedTime.ms = ms; \ 1329 cb_data.args.hipEventElapsedTime.start = start; \ 1330 cb_data.args.hipEventElapsedTime.stop = stop; \ 1333 #define INIT_hipDevicePrimaryCtxReset_CB_ARGS_DATA(cb_data) { \ 1334 cb_data.args.hipDevicePrimaryCtxReset.dev = dev; \ 1337 #define INIT_hipEventDestroy_CB_ARGS_DATA(cb_data) { \ 1338 cb_data.args.hipEventDestroy.event = event; \ 1341 #define INIT_hipCtxPopCurrent_CB_ARGS_DATA(cb_data) { \ 1342 cb_data.args.hipCtxPopCurrent.ctx = ctx; \ 1345 #define INIT_hipGetSymbolAddress_CB_ARGS_DATA(cb_data) { \ 1348 #define INIT_hipHostGetFlags_CB_ARGS_DATA(cb_data) { \ 1349 cb_data.args.hipHostGetFlags.flagsPtr = flagsPtr; \ 1350 cb_data.args.hipHostGetFlags.hostPtr = hostPtr; \ 1353 #define INIT_hipHostMalloc_CB_ARGS_DATA(cb_data) { \ 1354 cb_data.args.hipHostMalloc.ptr = ptr; \ 1355 cb_data.args.hipHostMalloc.size = sizeBytes; \ 1356 cb_data.args.hipHostMalloc.flags = flags; \ 1359 #define INIT_hipDriverGetVersion_CB_ARGS_DATA(cb_data) { \ 1360 cb_data.args.hipDriverGetVersion.driverVersion = driverVersion; \ 1363 #define INIT_hipMemGetInfo_CB_ARGS_DATA(cb_data) { \ 1364 cb_data.args.hipMemGetInfo.free = free; \ 1365 cb_data.args.hipMemGetInfo.total = total; \ 1368 #define INIT_hipDeviceReset_CB_ARGS_DATA(cb_data) { \ 1371 #define INIT_hipMemset_CB_ARGS_DATA(cb_data) { \ 1372 cb_data.args.hipMemset.dst = dst; \ 1373 cb_data.args.hipMemset.value = value; \ 1374 cb_data.args.hipMemset.sizeBytes = sizeBytes; \ 1377 #define INIT_hipMemsetD8_CB_ARGS_DATA(cb_data) { \ 1378 cb_data.args.hipMemsetD8.dest = dst; \ 1379 cb_data.args.hipMemsetD8.value = value; \ 1380 cb_data.args.hipMemsetD8.sizeBytes = sizeBytes; \ 1383 #define INIT_hipHostRegister_CB_ARGS_DATA(cb_data) { \ 1384 cb_data.args.hipHostRegister.hostPtr = hostPtr; \ 1385 cb_data.args.hipHostRegister.sizeBytes = sizeBytes; \ 1386 cb_data.args.hipHostRegister.flags = flags; \ 1389 #define INIT_hipCtxSetSharedMemConfig_CB_ARGS_DATA(cb_data) { \ 1390 cb_data.args.hipCtxSetSharedMemConfig.config = config; \ 1393 #define INIT_hipArray3DCreate_CB_ARGS_DATA(cb_data) { \ 1394 cb_data.args.hipArray3DCreate.array = array; \ 1395 cb_data.args.hipArray3DCreate.pAllocateArray = pAllocateArray; \ 1398 #define INIT_hipIpcOpenMemHandle_CB_ARGS_DATA(cb_data) { \ 1399 cb_data.args.hipIpcOpenMemHandle.devPtr = devPtr; \ 1400 cb_data.args.hipIpcOpenMemHandle.handle = handle; \ 1401 cb_data.args.hipIpcOpenMemHandle.flags = flags; \ 1404 #define INIT_hipGetLastError_CB_ARGS_DATA(cb_data) { \ 1407 #define INIT_hipCtxDestroy_CB_ARGS_DATA(cb_data) { \ 1408 cb_data.args.hipCtxDestroy.ctx = ctx; \ 1411 #define INIT_hipDeviceGetSharedMemConfig_CB_ARGS_DATA(cb_data) { \ 1412 cb_data.args.hipDeviceGetSharedMemConfig.pConfig = pConfig; \ 1415 #define INIT_hipSetDeviceFlags_CB_ARGS_DATA(cb_data) { \ 1416 cb_data.args.hipSetDeviceFlags.flags = flags; \ 1419 #define INIT_hipHccModuleLaunchKernel_CB_ARGS_DATA(cb_data) { \ 1420 cb_data.args.hipHccModuleLaunchKernel.f = f; \ 1421 cb_data.args.hipHccModuleLaunchKernel.globalWorkSizeX = globalWorkSizeX; \ 1422 cb_data.args.hipHccModuleLaunchKernel.globalWorkSizeY = globalWorkSizeY; \ 1423 cb_data.args.hipHccModuleLaunchKernel.globalWorkSizeZ = globalWorkSizeZ; \ 1424 cb_data.args.hipHccModuleLaunchKernel.localWorkSizeX = localWorkSizeX; \ 1425 cb_data.args.hipHccModuleLaunchKernel.localWorkSizeY = localWorkSizeY; \ 1426 cb_data.args.hipHccModuleLaunchKernel.localWorkSizeZ = localWorkSizeZ; \ 1427 cb_data.args.hipHccModuleLaunchKernel.sharedMemBytes = sharedMemBytes; \ 1428 cb_data.args.hipHccModuleLaunchKernel.hStream = hStream; \ 1429 cb_data.args.hipHccModuleLaunchKernel.kernelParams = kernelParams; \ 1430 cb_data.args.hipHccModuleLaunchKernel.extra = extra; \ 1431 cb_data.args.hipHccModuleLaunchKernel.startEvent = startEvent; \ 1432 cb_data.args.hipHccModuleLaunchKernel.stopEvent = stopEvent; \ 1435 #define INIT_hipFree_CB_ARGS_DATA(cb_data) { \ 1436 cb_data.args.hipFree.ptr = ptr; \ 1439 #define INIT_hipDeviceGetAttribute_CB_ARGS_DATA(cb_data) { \ 1440 cb_data.args.hipDeviceGetAttribute.pi = pi; \ 1441 cb_data.args.hipDeviceGetAttribute.attr = attr; \ 1442 cb_data.args.hipDeviceGetAttribute.deviceId = device; \ 1445 #define INIT_hipMemcpyDtoH_CB_ARGS_DATA(cb_data) { \ 1446 cb_data.args.hipMemcpyDtoH.dst = dst; \ 1447 cb_data.args.hipMemcpyDtoH.src = src; \ 1448 cb_data.args.hipMemcpyDtoH.sizeBytes = sizeBytes; \ 1451 #define INIT_hipCtxDisablePeerAccess_CB_ARGS_DATA(cb_data) { \ 1452 cb_data.args.hipCtxDisablePeerAccess.peerCtx = peerCtx; \ 1455 #define INIT_hipDeviceGetByPCIBusId_CB_ARGS_DATA(cb_data) { \ 1456 cb_data.args.hipDeviceGetByPCIBusId.device = device; \ 1457 cb_data.args.hipDeviceGetByPCIBusId.pciBusId = pciBusId; \ 1460 #define INIT_hipIpcGetMemHandle_CB_ARGS_DATA(cb_data) { \ 1461 cb_data.args.hipIpcGetMemHandle.handle = handle; \ 1462 cb_data.args.hipIpcGetMemHandle.devPtr = devPtr; \ 1465 #define INIT_hipMemcpyHtoDAsync_CB_ARGS_DATA(cb_data) { \ 1466 cb_data.args.hipMemcpyHtoDAsync.dst = dst; \ 1467 cb_data.args.hipMemcpyHtoDAsync.src = src; \ 1468 cb_data.args.hipMemcpyHtoDAsync.sizeBytes = sizeBytes; \ 1469 cb_data.args.hipMemcpyHtoDAsync.stream = stream; \ 1472 #define INIT_hipCtxGetDevice_CB_ARGS_DATA(cb_data) { \ 1473 cb_data.args.hipCtxGetDevice.device = device; \ 1476 #define INIT_hipMemset3D_CB_ARGS_DATA(cb_data) { \ 1477 cb_data.args.hipMemset3D.pitchedDevPtr = pitchedDevPtr; \ 1478 cb_data.args.hipMemset3D.value = value; \ 1479 cb_data.args.hipMemset3D.extent = extent; \ 1482 #define INIT_hipModuleLoadData_CB_ARGS_DATA(cb_data) { \ 1483 cb_data.args.hipModuleLoadData.module = module; \ 1484 cb_data.args.hipModuleLoadData.image = image; \ 1487 #define INIT_hipDeviceTotalMem_CB_ARGS_DATA(cb_data) { \ 1488 cb_data.args.hipDeviceTotalMem.bytes = bytes; \ 1489 cb_data.args.hipDeviceTotalMem.device = device; \ 1492 #define INIT_hipCtxSetCurrent_CB_ARGS_DATA(cb_data) { \ 1493 cb_data.args.hipCtxSetCurrent.ctx = ctx; \ 1496 #define INIT_hipGetErrorString_CB_ARGS_DATA(cb_data) { \ 1497 cb_data.args.hipGetErrorString.hipError = hip_error; \ 1500 #define INIT_hipDevicePrimaryCtxRetain_CB_ARGS_DATA(cb_data) { \ 1501 cb_data.args.hipDevicePrimaryCtxRetain.pctx = pctx; \ 1502 cb_data.args.hipDevicePrimaryCtxRetain.dev = dev; \ 1505 #define INIT_hipDeviceDisablePeerAccess_CB_ARGS_DATA(cb_data) { \ 1506 cb_data.args.hipDeviceDisablePeerAccess.peerDeviceId = peerDeviceId; \ 1509 #define INIT_hipStreamCreateWithFlags_CB_ARGS_DATA(cb_data) { \ 1510 cb_data.args.hipStreamCreateWithFlags.stream = stream; \ 1511 cb_data.args.hipStreamCreateWithFlags.flags = flags; \ 1514 #define INIT_hipMemcpyFromArray_CB_ARGS_DATA(cb_data) { \ 1515 cb_data.args.hipMemcpyFromArray.dst = dst; \ 1516 cb_data.args.hipMemcpyFromArray.srcArray = srcArray; \ 1517 cb_data.args.hipMemcpyFromArray.wOffset = wOffset; \ 1518 cb_data.args.hipMemcpyFromArray.hOffset = hOffset; \ 1519 cb_data.args.hipMemcpyFromArray.count = count; \ 1520 cb_data.args.hipMemcpyFromArray.kind = kind; \ 1523 #define INIT_hipMemcpy2DAsync_CB_ARGS_DATA(cb_data) { \ 1524 cb_data.args.hipMemcpy2DAsync.dst = dst; \ 1525 cb_data.args.hipMemcpy2DAsync.dpitch = dpitch; \ 1526 cb_data.args.hipMemcpy2DAsync.src = src; \ 1527 cb_data.args.hipMemcpy2DAsync.spitch = spitch; \ 1528 cb_data.args.hipMemcpy2DAsync.width = width; \ 1529 cb_data.args.hipMemcpy2DAsync.height = height; \ 1530 cb_data.args.hipMemcpy2DAsync.kind = kind; \ 1531 cb_data.args.hipMemcpy2DAsync.stream = stream; \ 1534 #define INIT_hipGetSymbolSize_CB_ARGS_DATA(cb_data) { \ 1537 #define INIT_hipEventCreateWithFlags_CB_ARGS_DATA(cb_data) { \ 1538 cb_data.args.hipEventCreateWithFlags.event = event; \ 1539 cb_data.args.hipEventCreateWithFlags.flags = flags; \ 1542 #define INIT_hipStreamQuery_CB_ARGS_DATA(cb_data) { \ 1543 cb_data.args.hipStreamQuery.stream = stream; \ 1546 #define INIT_hipDeviceGetPCIBusId_CB_ARGS_DATA(cb_data) { \ 1547 cb_data.args.hipDeviceGetPCIBusId.pciBusId = pciBusId; \ 1548 cb_data.args.hipDeviceGetPCIBusId.len = len; \ 1549 cb_data.args.hipDeviceGetPCIBusId.device = device; \ 1552 #define INIT_hipMemcpy_CB_ARGS_DATA(cb_data) { \ 1553 cb_data.args.hipMemcpy.dst = dst; \ 1554 cb_data.args.hipMemcpy.src = src; \ 1555 cb_data.args.hipMemcpy.sizeBytes = sizeBytes; \ 1556 cb_data.args.hipMemcpy.kind = kind; \ 1559 #define INIT_hipPeekAtLastError_CB_ARGS_DATA(cb_data) { \ 1562 #define INIT_hipStreamAddCallback_CB_ARGS_DATA(cb_data) { \ 1563 cb_data.args.hipStreamAddCallback.stream = stream; \ 1564 cb_data.args.hipStreamAddCallback.callback = callback; \ 1565 cb_data.args.hipStreamAddCallback.userData = userData; \ 1566 cb_data.args.hipStreamAddCallback.flags = flags; \ 1569 #define INIT_hipMemcpyToArray_CB_ARGS_DATA(cb_data) { \ 1570 cb_data.args.hipMemcpyToArray.dst = dst; \ 1571 cb_data.args.hipMemcpyToArray.wOffset = wOffset; \ 1572 cb_data.args.hipMemcpyToArray.hOffset = hOffset; \ 1573 cb_data.args.hipMemcpyToArray.src = src; \ 1574 cb_data.args.hipMemcpyToArray.count = count; \ 1575 cb_data.args.hipMemcpyToArray.kind = kind; \ 1578 #define INIT_hipMemsetD32_CB_ARGS_DATA(cb_data) { \ 1579 cb_data.args.hipMemsetD32.dest = dst; \ 1580 cb_data.args.hipMemsetD32.value = value; \ 1581 cb_data.args.hipMemsetD32.count = count; \ 1584 #define INIT_hipDeviceSynchronize_CB_ARGS_DATA(cb_data) { \ 1587 #define INIT_hipDeviceGetCacheConfig_CB_ARGS_DATA(cb_data) { \ 1588 cb_data.args.hipDeviceGetCacheConfig.cacheConfig = cacheConfig; \ 1591 #define INIT_hipMalloc3D_CB_ARGS_DATA(cb_data) { \ 1592 cb_data.args.hipMalloc3D.pitchedDevPtr = pitchedDevPtr; \ 1593 cb_data.args.hipMalloc3D.extent = extent; \ 1596 #define INIT_hipPointerGetAttributes_CB_ARGS_DATA(cb_data) { \ 1597 cb_data.args.hipPointerGetAttributes.attributes = attributes; \ 1598 cb_data.args.hipPointerGetAttributes.ptr = ptr; \ 1601 #define INIT_hipMemsetAsync_CB_ARGS_DATA(cb_data) { \ 1602 cb_data.args.hipMemsetAsync.dst = dst; \ 1603 cb_data.args.hipMemsetAsync.value = value; \ 1604 cb_data.args.hipMemsetAsync.sizeBytes = sizeBytes; \ 1605 cb_data.args.hipMemsetAsync.stream = stream; \ 1608 #define INIT_hipMemcpyToSymbol_CB_ARGS_DATA(cb_data) { \ 1611 #define INIT_hipCtxPushCurrent_CB_ARGS_DATA(cb_data) { \ 1612 cb_data.args.hipCtxPushCurrent.ctx = ctx; \ 1615 #define INIT_hipMemcpyPeer_CB_ARGS_DATA(cb_data) { \ 1616 cb_data.args.hipMemcpyPeer.dst = dst; \ 1617 cb_data.args.hipMemcpyPeer.dstDeviceId = dstDevice; \ 1618 cb_data.args.hipMemcpyPeer.src = src; \ 1619 cb_data.args.hipMemcpyPeer.srcDeviceId = srcDevice; \ 1620 cb_data.args.hipMemcpyPeer.sizeBytes = sizeBytes; \ 1623 #define INIT_hipEventSynchronize_CB_ARGS_DATA(cb_data) { \ 1624 cb_data.args.hipEventSynchronize.event = event; \ 1627 #define INIT_hipMemcpyDtoDAsync_CB_ARGS_DATA(cb_data) { \ 1628 cb_data.args.hipMemcpyDtoDAsync.dst = dst; \ 1629 cb_data.args.hipMemcpyDtoDAsync.src = src; \ 1630 cb_data.args.hipMemcpyDtoDAsync.sizeBytes = sizeBytes; \ 1631 cb_data.args.hipMemcpyDtoDAsync.stream = stream; \ 1634 #define INIT_hipExtMallocWithFlags_CB_ARGS_DATA(cb_data) { \ 1635 cb_data.args.hipExtMallocWithFlags.ptr = ptr; \ 1636 cb_data.args.hipExtMallocWithFlags.sizeBytes = sizeBytes; \ 1637 cb_data.args.hipExtMallocWithFlags.flags = flags; \ 1640 #define INIT_hipCtxEnablePeerAccess_CB_ARGS_DATA(cb_data) { \ 1641 cb_data.args.hipCtxEnablePeerAccess.peerCtx = peerCtx; \ 1642 cb_data.args.hipCtxEnablePeerAccess.flags = flags; \ 1645 #define INIT_hipMemcpyDtoHAsync_CB_ARGS_DATA(cb_data) { \ 1646 cb_data.args.hipMemcpyDtoHAsync.dst = dst; \ 1647 cb_data.args.hipMemcpyDtoHAsync.src = src; \ 1648 cb_data.args.hipMemcpyDtoHAsync.sizeBytes = sizeBytes; \ 1649 cb_data.args.hipMemcpyDtoHAsync.stream = stream; \ 1652 #define INIT_hipModuleLaunchKernel_CB_ARGS_DATA(cb_data) { \ 1653 cb_data.args.hipModuleLaunchKernel.f = f; \ 1654 cb_data.args.hipModuleLaunchKernel.gridDimX = gridDimX; \ 1655 cb_data.args.hipModuleLaunchKernel.gridDimY = gridDimY; \ 1656 cb_data.args.hipModuleLaunchKernel.gridDimZ = gridDimZ; \ 1657 cb_data.args.hipModuleLaunchKernel.blockDimX = blockDimX; \ 1658 cb_data.args.hipModuleLaunchKernel.blockDimY = blockDimY; \ 1659 cb_data.args.hipModuleLaunchKernel.blockDimZ = blockDimZ; \ 1660 cb_data.args.hipModuleLaunchKernel.sharedMemBytes = sharedMemBytes; \ 1661 cb_data.args.hipModuleLaunchKernel.stream = hStream; \ 1662 cb_data.args.hipModuleLaunchKernel.kernelParams = kernelParams; \ 1663 cb_data.args.hipModuleLaunchKernel.extra = extra; \ 1666 #define INIT_hipModuleGetTexRef_CB_ARGS_DATA(cb_data) { \ 1667 cb_data.args.hipModuleGetTexRef.texRef = texRef; \ 1668 cb_data.args.hipModuleGetTexRef.hmod = hmod; \ 1669 cb_data.args.hipModuleGetTexRef.name = name; \ 1672 #define INIT_hipDeviceGetLimit_CB_ARGS_DATA(cb_data) { \ 1673 cb_data.args.hipDeviceGetLimit.pValue = pValue; \ 1674 cb_data.args.hipDeviceGetLimit.limit = limit; \ 1677 #define INIT_hipModuleLoadDataEx_CB_ARGS_DATA(cb_data) { \ 1678 cb_data.args.hipModuleLoadDataEx.module = module; \ 1679 cb_data.args.hipModuleLoadDataEx.image = image; \ 1680 cb_data.args.hipModuleLoadDataEx.numOptions = numOptions; \ 1681 cb_data.args.hipModuleLoadDataEx.options = options; \ 1682 cb_data.args.hipModuleLoadDataEx.optionValues = optionValues; \ 1685 #define INIT_hipRuntimeGetVersion_CB_ARGS_DATA(cb_data) { \ 1686 cb_data.args.hipRuntimeGetVersion.runtimeVersion = runtimeVersion; \ 1689 #define INIT_hipGetDeviceProperties_CB_ARGS_DATA(cb_data) { \ 1690 cb_data.args.hipGetDeviceProperties.prop = props; \ 1691 cb_data.args.hipGetDeviceProperties.deviceId = device; \ 1694 #define INIT_hipFreeArray_CB_ARGS_DATA(cb_data) { \ 1695 cb_data.args.hipFreeArray.array = array; \ 1698 #define INIT_hipDevicePrimaryCtxRelease_CB_ARGS_DATA(cb_data) { \ 1699 cb_data.args.hipDevicePrimaryCtxRelease.dev = dev; \ 1702 #define INIT_hipHostGetDevicePointer_CB_ARGS_DATA(cb_data) { \ 1703 cb_data.args.hipHostGetDevicePointer.devPtr = devicePointer; \ 1704 cb_data.args.hipHostGetDevicePointer.hstPtr = hostPointer; \ 1705 cb_data.args.hipHostGetDevicePointer.flags = flags; \ 1708 #define INIT_hipMemcpyParam2D_CB_ARGS_DATA(cb_data) { \ 1709 cb_data.args.hipMemcpyParam2D.pCopy = pCopy; \ 1712 #define INIT_hipModuleGetFunction_CB_ARGS_DATA(cb_data) { \ 1713 cb_data.args.hipModuleGetFunction.function = hfunc; \ 1714 cb_data.args.hipModuleGetFunction.module = hmod; \ 1715 cb_data.args.hipModuleGetFunction.kname = name; \ 1718 #define INIT_hipMemsetD32Async_CB_ARGS_DATA(cb_data) { \ 1719 cb_data.args.hipMemsetD32Async.dst = dst; \ 1720 cb_data.args.hipMemsetD32Async.value = value; \ 1721 cb_data.args.hipMemsetD32Async.count = count; \ 1722 cb_data.args.hipMemsetD32Async.stream = stream; \ 1725 #define INIT_hipGetDevice_CB_ARGS_DATA(cb_data) { \ 1726 cb_data.args.hipGetDevice.deviceId = deviceId; \ 1729 #define INIT_hipGetDeviceCount_CB_ARGS_DATA(cb_data) { \ 1730 cb_data.args.hipGetDeviceCount.count = count; \ 1732 #define INIT_CB_ARGS_DATA(cb_id, cb_data) INIT_##cb_id##_CB_ARGS_DATA(cb_data) 1736 const char* hipApiString(hip_api_id_t
id,
const hip_api_data_t* data) {
1737 std::ostringstream oss;
1739 case HIP_API_ID_hipStreamCreateWithPriority:
1740 oss <<
"hipStreamCreateWithPriority(" 1741 <<
" stream=" << data->args.hipStreamCreateWithPriority.stream <<
"," 1742 <<
" flags=" << data->args.hipStreamCreateWithPriority.flags <<
"," 1743 <<
" priority=" << data->args.hipStreamCreateWithPriority.priority
1746 case HIP_API_ID_hipMemcpyToSymbolAsync:
1747 oss <<
"hipMemcpyToSymbolAsync(" 1748 <<
" symbolName=" << data->args.hipMemcpyToSymbolAsync.symbolName <<
"," 1749 <<
" src=" << data->args.hipMemcpyToSymbolAsync.src <<
"," 1750 <<
" sizeBytes=" << data->args.hipMemcpyToSymbolAsync.sizeBytes <<
"," 1751 <<
" offset=" << data->args.hipMemcpyToSymbolAsync.offset <<
"," 1752 <<
" kind=" << data->args.hipMemcpyToSymbolAsync.kind <<
"," 1753 <<
" stream=" << data->args.hipMemcpyToSymbolAsync.stream
1756 case HIP_API_ID_hipMallocPitch:
1757 oss <<
"hipMallocPitch(" 1758 <<
" ptr=" << data->args.hipMallocPitch.ptr <<
"," 1759 <<
" pitch=" << data->args.hipMallocPitch.pitch <<
"," 1760 <<
" width=" << data->args.hipMallocPitch.width <<
"," 1761 <<
" height=" << data->args.hipMallocPitch.height
1764 case HIP_API_ID_hipMalloc:
1766 <<
" ptr=" << data->args.hipMalloc.ptr <<
"," 1767 <<
" size=" << data->args.hipMalloc.size
1770 case HIP_API_ID_hipDeviceGetName:
1771 oss <<
"hipDeviceGetName(" 1772 <<
" name=" << data->args.hipDeviceGetName.name <<
"," 1773 <<
" len=" << data->args.hipDeviceGetName.len <<
"," 1774 <<
" device=" << data->args.hipDeviceGetName.device
1777 case HIP_API_ID_hipEventRecord:
1778 oss <<
"hipEventRecord(" 1779 <<
" event=" << data->args.hipEventRecord.event <<
"," 1780 <<
" stream=" << data->args.hipEventRecord.stream
1783 case HIP_API_ID_hipCtxSynchronize:
1784 oss <<
"hipCtxSynchronize(" 1787 case HIP_API_ID_hipSetDevice:
1788 oss <<
"hipSetDevice(" 1789 <<
" deviceId=" << data->args.hipSetDevice.deviceId
1792 case HIP_API_ID_hipCtxGetApiVersion:
1793 oss <<
"hipCtxGetApiVersion(" 1794 <<
" ctx=" << data->args.hipCtxGetApiVersion.ctx <<
"," 1795 <<
" apiVersion=" << data->args.hipCtxGetApiVersion.apiVersion
1798 case HIP_API_ID_hipSetupArgument:
1799 oss <<
"hipSetupArgument(" 1800 <<
" arg=" << data->args.hipSetupArgument.arg <<
"," 1801 <<
" size=" << data->args.hipSetupArgument.size <<
"," 1802 <<
" offset=" << data->args.hipSetupArgument.offset
1805 case HIP_API_ID_hipMemcpyFromSymbolAsync:
1806 oss <<
"hipMemcpyFromSymbolAsync(" 1807 <<
" dst=" << data->args.hipMemcpyFromSymbolAsync.dst <<
"," 1808 <<
" symbolName=" << data->args.hipMemcpyFromSymbolAsync.symbolName <<
"," 1809 <<
" sizeBytes=" << data->args.hipMemcpyFromSymbolAsync.sizeBytes <<
"," 1810 <<
" offset=" << data->args.hipMemcpyFromSymbolAsync.offset <<
"," 1811 <<
" kind=" << data->args.hipMemcpyFromSymbolAsync.kind <<
"," 1812 <<
" stream=" << data->args.hipMemcpyFromSymbolAsync.stream
1815 case HIP_API_ID_hipMemcpyDtoD:
1816 oss <<
"hipMemcpyDtoD(" 1817 <<
" dst=" << data->args.hipMemcpyDtoD.dst <<
"," 1818 <<
" src=" << data->args.hipMemcpyDtoD.src <<
"," 1819 <<
" sizeBytes=" << data->args.hipMemcpyDtoD.sizeBytes
1822 case HIP_API_ID_hipHostFree:
1823 oss <<
"hipHostFree(" 1824 <<
" ptr=" << data->args.hipHostFree.ptr
1827 case HIP_API_ID_hipMemcpy2DToArray:
1828 oss <<
"hipMemcpy2DToArray(" 1829 <<
" dst=" << data->args.hipMemcpy2DToArray.dst <<
"," 1830 <<
" wOffset=" << data->args.hipMemcpy2DToArray.wOffset <<
"," 1831 <<
" hOffset=" << data->args.hipMemcpy2DToArray.hOffset <<
"," 1832 <<
" src=" << data->args.hipMemcpy2DToArray.src <<
"," 1833 <<
" spitch=" << data->args.hipMemcpy2DToArray.spitch <<
"," 1834 <<
" width=" << data->args.hipMemcpy2DToArray.width <<
"," 1835 <<
" height=" << data->args.hipMemcpy2DToArray.height <<
"," 1836 <<
" kind=" << data->args.hipMemcpy2DToArray.kind
1839 case HIP_API_ID_hipCtxGetCacheConfig:
1840 oss <<
"hipCtxGetCacheConfig(" 1841 <<
" cacheConfig=" << data->args.hipCtxGetCacheConfig.cacheConfig
1844 case HIP_API_ID_hipStreamWaitEvent:
1845 oss <<
"hipStreamWaitEvent(" 1846 <<
" stream=" << data->args.hipStreamWaitEvent.stream <<
"," 1847 <<
" event=" << data->args.hipStreamWaitEvent.event <<
"," 1848 <<
" flags=" << data->args.hipStreamWaitEvent.flags
1851 case HIP_API_ID_hipDeviceGetStreamPriorityRange:
1852 oss <<
"hipDeviceGetStreamPriorityRange(" 1853 <<
" leastPriority=" << data->args.hipDeviceGetStreamPriorityRange.leastPriority <<
"," 1854 <<
" greatestPriority=" << data->args.hipDeviceGetStreamPriorityRange.greatestPriority
1857 case HIP_API_ID_hipModuleLoad:
1858 oss <<
"hipModuleLoad(" 1859 <<
" module=" << data->args.hipModuleLoad.module <<
"," 1860 <<
" fname=" << data->args.hipModuleLoad.fname
1863 case HIP_API_ID_hipDevicePrimaryCtxSetFlags:
1864 oss <<
"hipDevicePrimaryCtxSetFlags(" 1865 <<
" dev=" << data->args.hipDevicePrimaryCtxSetFlags.dev <<
"," 1866 <<
" flags=" << data->args.hipDevicePrimaryCtxSetFlags.flags
1869 case HIP_API_ID_hipMemcpyAsync:
1870 oss <<
"hipMemcpyAsync(" 1871 <<
" dst=" << data->args.hipMemcpyAsync.dst <<
"," 1872 <<
" src=" << data->args.hipMemcpyAsync.src <<
"," 1873 <<
" sizeBytes=" << data->args.hipMemcpyAsync.sizeBytes <<
"," 1874 <<
" kind=" << data->args.hipMemcpyAsync.kind <<
"," 1875 <<
" stream=" << data->args.hipMemcpyAsync.stream
1878 case HIP_API_ID_hipMalloc3DArray:
1879 oss <<
"hipMalloc3DArray(" 1880 <<
" array=" << data->args.hipMalloc3DArray.array <<
"," 1881 <<
" desc=" << data->args.hipMalloc3DArray.desc <<
"," 1882 <<
" extent=" << data->args.hipMalloc3DArray.extent <<
"," 1883 <<
" flags=" << data->args.hipMalloc3DArray.flags
1886 case HIP_API_ID_hipStreamCreate:
1887 oss <<
"hipStreamCreate(" 1888 <<
" stream=" << data->args.hipStreamCreate.stream
1891 case HIP_API_ID_hipCtxGetCurrent:
1892 oss <<
"hipCtxGetCurrent(" 1893 <<
" ctx=" << data->args.hipCtxGetCurrent.ctx
1896 case HIP_API_ID_hipDevicePrimaryCtxGetState:
1897 oss <<
"hipDevicePrimaryCtxGetState(" 1898 <<
" dev=" << data->args.hipDevicePrimaryCtxGetState.dev <<
"," 1899 <<
" flags=" << data->args.hipDevicePrimaryCtxGetState.flags <<
"," 1900 <<
" active=" << data->args.hipDevicePrimaryCtxGetState.active
1903 case HIP_API_ID_hipEventQuery:
1904 oss <<
"hipEventQuery(" 1905 <<
" event=" << data->args.hipEventQuery.event
1908 case HIP_API_ID_hipEventCreate:
1909 oss <<
"hipEventCreate(" 1910 <<
" event=" << data->args.hipEventCreate.event
1913 case HIP_API_ID_hipMemGetAddressRange:
1914 oss <<
"hipMemGetAddressRange(" 1915 <<
" pbase=" << data->args.hipMemGetAddressRange.pbase <<
"," 1916 <<
" psize=" << data->args.hipMemGetAddressRange.psize <<
"," 1917 <<
" dptr=" << data->args.hipMemGetAddressRange.dptr
1920 case HIP_API_ID_hipMemcpyFromSymbol:
1921 oss <<
"hipMemcpyFromSymbol(" 1922 <<
" dst=" << data->args.hipMemcpyFromSymbol.dst <<
"," 1923 <<
" symbolName=" << data->args.hipMemcpyFromSymbol.symbolName <<
"," 1924 <<
" sizeBytes=" << data->args.hipMemcpyFromSymbol.sizeBytes <<
"," 1925 <<
" offset=" << data->args.hipMemcpyFromSymbol.offset <<
"," 1926 <<
" kind=" << data->args.hipMemcpyFromSymbol.kind
1929 case HIP_API_ID_hipArrayCreate:
1930 oss <<
"hipArrayCreate(" 1931 <<
" pHandle=" << data->args.hipArrayCreate.pHandle <<
"," 1932 <<
" pAllocateArray=" << data->args.hipArrayCreate.pAllocateArray
1935 case HIP_API_ID_hipStreamGetFlags:
1936 oss <<
"hipStreamGetFlags(" 1937 <<
" stream=" << data->args.hipStreamGetFlags.stream <<
"," 1938 <<
" flags=" << data->args.hipStreamGetFlags.flags
1941 case HIP_API_ID_hipMallocArray:
1942 oss <<
"hipMallocArray(" 1943 <<
" array=" << data->args.hipMallocArray.array <<
"," 1944 <<
" desc=" << data->args.hipMallocArray.desc <<
"," 1945 <<
" width=" << data->args.hipMallocArray.width <<
"," 1946 <<
" height=" << data->args.hipMallocArray.height <<
"," 1947 <<
" flags=" << data->args.hipMallocArray.flags
1950 case HIP_API_ID_hipCtxGetSharedMemConfig:
1951 oss <<
"hipCtxGetSharedMemConfig(" 1952 <<
" pConfig=" << data->args.hipCtxGetSharedMemConfig.pConfig
1955 case HIP_API_ID_hipMemPtrGetInfo:
1956 oss <<
"hipMemPtrGetInfo(" 1957 <<
" ptr=" << data->args.hipMemPtrGetInfo.ptr <<
"," 1958 <<
" size=" << data->args.hipMemPtrGetInfo.size
1961 case HIP_API_ID_hipCtxGetFlags:
1962 oss <<
"hipCtxGetFlags(" 1963 <<
" flags=" << data->args.hipCtxGetFlags.flags
1966 case HIP_API_ID_hipStreamDestroy:
1967 oss <<
"hipStreamDestroy(" 1968 <<
" stream=" << data->args.hipStreamDestroy.stream
1971 case HIP_API_ID_hipMemset3DAsync:
1972 oss <<
"hipMemset3DAsync(" 1973 <<
" pitchedDevPtr=" << data->args.hipMemset3DAsync.pitchedDevPtr <<
"," 1974 <<
" value=" << data->args.hipMemset3DAsync.value <<
"," 1975 <<
" extent=" << data->args.hipMemset3DAsync.extent <<
"," 1976 <<
" stream=" << data->args.hipMemset3DAsync.stream
1979 case HIP_API_ID_hipMemcpy3D:
1980 oss <<
"hipMemcpy3D(" 1981 <<
" p=" << data->args.hipMemcpy3D.p
1984 case HIP_API_ID_hipInit:
1986 <<
" flags=" << data->args.hipInit.flags
1989 case HIP_API_ID_hipMemcpyAtoH:
1990 oss <<
"hipMemcpyAtoH(" 1991 <<
" dst=" << data->args.hipMemcpyAtoH.dst <<
"," 1992 <<
" srcArray=" << data->args.hipMemcpyAtoH.srcArray <<
"," 1993 <<
" srcOffset=" << data->args.hipMemcpyAtoH.srcOffset <<
"," 1994 <<
" count=" << data->args.hipMemcpyAtoH.count
1997 case HIP_API_ID_hipStreamGetPriority:
1998 oss <<
"hipStreamGetPriority(" 1999 <<
" stream=" << data->args.hipStreamGetPriority.stream <<
"," 2000 <<
" priority=" << data->args.hipStreamGetPriority.priority
2003 case HIP_API_ID_hipMemset2D:
2004 oss <<
"hipMemset2D(" 2005 <<
" dst=" << data->args.hipMemset2D.dst <<
"," 2006 <<
" pitch=" << data->args.hipMemset2D.pitch <<
"," 2007 <<
" value=" << data->args.hipMemset2D.value <<
"," 2008 <<
" width=" << data->args.hipMemset2D.width <<
"," 2009 <<
" height=" << data->args.hipMemset2D.height
2012 case HIP_API_ID_hipMemset2DAsync:
2013 oss <<
"hipMemset2DAsync(" 2014 <<
" dst=" << data->args.hipMemset2DAsync.dst <<
"," 2015 <<
" pitch=" << data->args.hipMemset2DAsync.pitch <<
"," 2016 <<
" value=" << data->args.hipMemset2DAsync.value <<
"," 2017 <<
" width=" << data->args.hipMemset2DAsync.width <<
"," 2018 <<
" height=" << data->args.hipMemset2DAsync.height <<
"," 2019 <<
" stream=" << data->args.hipMemset2DAsync.stream
2022 case HIP_API_ID_hipDeviceCanAccessPeer:
2023 oss <<
"hipDeviceCanAccessPeer(" 2024 <<
" canAccessPeer=" << data->args.hipDeviceCanAccessPeer.canAccessPeer <<
"," 2025 <<
" deviceId=" << data->args.hipDeviceCanAccessPeer.deviceId <<
"," 2026 <<
" peerDeviceId=" << data->args.hipDeviceCanAccessPeer.peerDeviceId
2029 case HIP_API_ID_hipDeviceEnablePeerAccess:
2030 oss <<
"hipDeviceEnablePeerAccess(" 2031 <<
" peerDeviceId=" << data->args.hipDeviceEnablePeerAccess.peerDeviceId <<
"," 2032 <<
" flags=" << data->args.hipDeviceEnablePeerAccess.flags
2035 case HIP_API_ID_hipModuleUnload:
2036 oss <<
"hipModuleUnload(" 2037 <<
" module=" << data->args.hipModuleUnload.module
2040 case HIP_API_ID_hipHostUnregister:
2041 oss <<
"hipHostUnregister(" 2042 <<
" hostPtr=" << data->args.hipHostUnregister.hostPtr
2045 case HIP_API_ID_hipProfilerStop:
2046 oss <<
"hipProfilerStop(" 2049 case HIP_API_ID_hipLaunchByPtr:
2050 oss <<
"hipLaunchByPtr(" 2051 <<
" func=" << data->args.hipLaunchByPtr.func
2054 case HIP_API_ID_hipStreamSynchronize:
2055 oss <<
"hipStreamSynchronize(" 2056 <<
" stream=" << data->args.hipStreamSynchronize.stream
2059 case HIP_API_ID_hipDeviceSetCacheConfig:
2060 oss <<
"hipDeviceSetCacheConfig(" 2061 <<
" cacheConfig=" << data->args.hipDeviceSetCacheConfig.cacheConfig
2064 case HIP_API_ID_hipGetErrorName:
2065 oss <<
"hipGetErrorName(" 2066 <<
" hip_error=" << data->args.hipGetErrorName.hip_error
2069 case HIP_API_ID_hipMemcpyHtoD:
2070 oss <<
"hipMemcpyHtoD(" 2071 <<
" dst=" << data->args.hipMemcpyHtoD.dst <<
"," 2072 <<
" src=" << data->args.hipMemcpyHtoD.src <<
"," 2073 <<
" sizeBytes=" << data->args.hipMemcpyHtoD.sizeBytes
2076 case HIP_API_ID_hipModuleGetGlobal:
2077 oss <<
"hipModuleGetGlobal(" 2078 <<
" dptr=" << data->args.hipModuleGetGlobal.dptr <<
"," 2079 <<
" bytes=" << data->args.hipModuleGetGlobal.bytes <<
"," 2080 <<
" hmod=" << data->args.hipModuleGetGlobal.hmod <<
"," 2081 <<
" name=" << data->args.hipModuleGetGlobal.name
2084 case HIP_API_ID_hipMemcpyHtoA:
2085 oss <<
"hipMemcpyHtoA(" 2086 <<
" dstArray=" << data->args.hipMemcpyHtoA.dstArray <<
"," 2087 <<
" dstOffset=" << data->args.hipMemcpyHtoA.dstOffset <<
"," 2088 <<
" srcHost=" << data->args.hipMemcpyHtoA.srcHost <<
"," 2089 <<
" count=" << data->args.hipMemcpyHtoA.count
2092 case HIP_API_ID_hipCtxCreate:
2093 oss <<
"hipCtxCreate(" 2094 <<
" ctx=" << data->args.hipCtxCreate.ctx <<
"," 2095 <<
" flags=" << data->args.hipCtxCreate.flags <<
"," 2096 <<
" device=" << data->args.hipCtxCreate.device
2099 case HIP_API_ID_hipMemcpy2D:
2100 oss <<
"hipMemcpy2D(" 2101 <<
" dst=" << data->args.hipMemcpy2D.dst <<
"," 2102 <<
" dpitch=" << data->args.hipMemcpy2D.dpitch <<
"," 2103 <<
" src=" << data->args.hipMemcpy2D.src <<
"," 2104 <<
" spitch=" << data->args.hipMemcpy2D.spitch <<
"," 2105 <<
" width=" << data->args.hipMemcpy2D.width <<
"," 2106 <<
" height=" << data->args.hipMemcpy2D.height <<
"," 2107 <<
" kind=" << data->args.hipMemcpy2D.kind
2110 case HIP_API_ID_hipIpcCloseMemHandle:
2111 oss <<
"hipIpcCloseMemHandle(" 2112 <<
" devPtr=" << data->args.hipIpcCloseMemHandle.devPtr
2115 case HIP_API_ID_hipChooseDevice:
2116 oss <<
"hipChooseDevice(" 2117 <<
" device=" << data->args.hipChooseDevice.device <<
"," 2118 <<
" prop=" << data->args.hipChooseDevice.prop
2121 case HIP_API_ID_hipDeviceSetSharedMemConfig:
2122 oss <<
"hipDeviceSetSharedMemConfig(" 2123 <<
" config=" << data->args.hipDeviceSetSharedMemConfig.config
2126 case HIP_API_ID_hipDeviceComputeCapability:
2127 oss <<
"hipDeviceComputeCapability(" 2128 <<
" major=" << data->args.hipDeviceComputeCapability.major <<
"," 2129 <<
" minor=" << data->args.hipDeviceComputeCapability.minor <<
"," 2130 <<
" device=" << data->args.hipDeviceComputeCapability.device
2133 case HIP_API_ID_hipDeviceGet:
2134 oss <<
"hipDeviceGet(" 2135 <<
" device=" << data->args.hipDeviceGet.device <<
"," 2136 <<
" ordinal=" << data->args.hipDeviceGet.ordinal
2139 case HIP_API_ID_hipProfilerStart:
2140 oss <<
"hipProfilerStart(" 2143 case HIP_API_ID_hipCtxSetCacheConfig:
2144 oss <<
"hipCtxSetCacheConfig(" 2145 <<
" cacheConfig=" << data->args.hipCtxSetCacheConfig.cacheConfig
2148 case HIP_API_ID_hipFuncSetCacheConfig:
2149 oss <<
"hipFuncSetCacheConfig(" 2150 <<
" func=" << data->args.hipFuncSetCacheConfig.func <<
"," 2151 <<
" config=" << data->args.hipFuncSetCacheConfig.config
2154 case HIP_API_ID_hipMemcpyPeerAsync:
2155 oss <<
"hipMemcpyPeerAsync(" 2156 <<
" dst=" << data->args.hipMemcpyPeerAsync.dst <<
"," 2157 <<
" dstDeviceId=" << data->args.hipMemcpyPeerAsync.dstDeviceId <<
"," 2158 <<
" src=" << data->args.hipMemcpyPeerAsync.src <<
"," 2159 <<
" srcDevice=" << data->args.hipMemcpyPeerAsync.srcDevice <<
"," 2160 <<
" sizeBytes=" << data->args.hipMemcpyPeerAsync.sizeBytes <<
"," 2161 <<
" stream=" << data->args.hipMemcpyPeerAsync.stream
2164 case HIP_API_ID_hipEventElapsedTime:
2165 oss <<
"hipEventElapsedTime(" 2166 <<
" ms=" << data->args.hipEventElapsedTime.ms <<
"," 2167 <<
" start=" << data->args.hipEventElapsedTime.start <<
"," 2168 <<
" stop=" << data->args.hipEventElapsedTime.stop
2171 case HIP_API_ID_hipDevicePrimaryCtxReset:
2172 oss <<
"hipDevicePrimaryCtxReset(" 2173 <<
" dev=" << data->args.hipDevicePrimaryCtxReset.dev
2176 case HIP_API_ID_hipEventDestroy:
2177 oss <<
"hipEventDestroy(" 2178 <<
" event=" << data->args.hipEventDestroy.event
2181 case HIP_API_ID_hipCtxPopCurrent:
2182 oss <<
"hipCtxPopCurrent(" 2183 <<
" ctx=" << data->args.hipCtxPopCurrent.ctx
2186 case HIP_API_ID_hipGetSymbolAddress:
2187 oss <<
"hipGetSymbolAddress(" 2188 <<
" devPtr=" << data->args.hipGetSymbolAddress.devPtr <<
"," 2189 <<
" symbolName=" << data->args.hipGetSymbolAddress.symbolName
2192 case HIP_API_ID_hipHostGetFlags:
2193 oss <<
"hipHostGetFlags(" 2194 <<
" flagsPtr=" << data->args.hipHostGetFlags.flagsPtr <<
"," 2195 <<
" hostPtr=" << data->args.hipHostGetFlags.hostPtr
2198 case HIP_API_ID_hipHostMalloc:
2199 oss <<
"hipHostMalloc(" 2200 <<
" ptr=" << data->args.hipHostMalloc.ptr <<
"," 2201 <<
" size=" << data->args.hipHostMalloc.size <<
"," 2202 <<
" flags=" << data->args.hipHostMalloc.flags
2205 case HIP_API_ID_hipDriverGetVersion:
2206 oss <<
"hipDriverGetVersion(" 2207 <<
" driverVersion=" << data->args.hipDriverGetVersion.driverVersion
2210 case HIP_API_ID_hipMemGetInfo:
2211 oss <<
"hipMemGetInfo(" 2212 <<
" free=" << data->args.hipMemGetInfo.free <<
"," 2213 <<
" total=" << data->args.hipMemGetInfo.total
2216 case HIP_API_ID_hipDeviceReset:
2217 oss <<
"hipDeviceReset(" 2220 case HIP_API_ID_hipMemset:
2222 <<
" dst=" << data->args.hipMemset.dst <<
"," 2223 <<
" value=" << data->args.hipMemset.value <<
"," 2224 <<
" sizeBytes=" << data->args.hipMemset.sizeBytes
2227 case HIP_API_ID_hipMemsetD8:
2228 oss <<
"hipMemsetD8(" 2229 <<
" dest=" << data->args.hipMemsetD8.dest <<
"," 2230 <<
" value=" << data->args.hipMemsetD8.value <<
"," 2231 <<
" sizeBytes=" << data->args.hipMemsetD8.sizeBytes
2234 case HIP_API_ID_hipHostRegister:
2235 oss <<
"hipHostRegister(" 2236 <<
" hostPtr=" << data->args.hipHostRegister.hostPtr <<
"," 2237 <<
" sizeBytes=" << data->args.hipHostRegister.sizeBytes <<
"," 2238 <<
" flags=" << data->args.hipHostRegister.flags
2241 case HIP_API_ID_hipCtxSetSharedMemConfig:
2242 oss <<
"hipCtxSetSharedMemConfig(" 2243 <<
" config=" << data->args.hipCtxSetSharedMemConfig.config
2246 case HIP_API_ID_hipArray3DCreate:
2247 oss <<
"hipArray3DCreate(" 2248 <<
" array=" << data->args.hipArray3DCreate.array <<
"," 2249 <<
" pAllocateArray=" << data->args.hipArray3DCreate.pAllocateArray
2252 case HIP_API_ID_hipIpcOpenMemHandle:
2253 oss <<
"hipIpcOpenMemHandle(" 2254 <<
" devPtr=" << data->args.hipIpcOpenMemHandle.devPtr <<
"," 2255 <<
" handle=" << data->args.hipIpcOpenMemHandle.handle <<
"," 2256 <<
" flags=" << data->args.hipIpcOpenMemHandle.flags
2259 case HIP_API_ID_hipGetLastError:
2260 oss <<
"hipGetLastError(" 2263 case HIP_API_ID_hipCtxDestroy:
2264 oss <<
"hipCtxDestroy(" 2265 <<
" ctx=" << data->args.hipCtxDestroy.ctx
2268 case HIP_API_ID_hipDeviceGetSharedMemConfig:
2269 oss <<
"hipDeviceGetSharedMemConfig(" 2270 <<
" pConfig=" << data->args.hipDeviceGetSharedMemConfig.pConfig
2273 case HIP_API_ID_hipSetDeviceFlags:
2274 oss <<
"hipSetDeviceFlags(" 2275 <<
" flags=" << data->args.hipSetDeviceFlags.flags
2278 case HIP_API_ID_hipHccModuleLaunchKernel:
2279 oss <<
"hipHccModuleLaunchKernel(" 2280 <<
" f=" << data->args.hipHccModuleLaunchKernel.f <<
"," 2281 <<
" globalWorkSizeX=" << data->args.hipHccModuleLaunchKernel.globalWorkSizeX <<
"," 2282 <<
" globalWorkSizeY=" << data->args.hipHccModuleLaunchKernel.globalWorkSizeY <<
"," 2283 <<
" globalWorkSizeZ=" << data->args.hipHccModuleLaunchKernel.globalWorkSizeZ <<
"," 2284 <<
" localWorkSizeX=" << data->args.hipHccModuleLaunchKernel.localWorkSizeX <<
"," 2285 <<
" localWorkSizeY=" << data->args.hipHccModuleLaunchKernel.localWorkSizeY <<
"," 2286 <<
" localWorkSizeZ=" << data->args.hipHccModuleLaunchKernel.localWorkSizeZ <<
"," 2287 <<
" sharedMemBytes=" << data->args.hipHccModuleLaunchKernel.sharedMemBytes <<
"," 2288 <<
" hStream=" << data->args.hipHccModuleLaunchKernel.hStream <<
"," 2289 <<
" kernelParams=" << data->args.hipHccModuleLaunchKernel.kernelParams <<
"," 2290 <<
" extra=" << data->args.hipHccModuleLaunchKernel.extra <<
"," 2291 <<
" startEvent=" << data->args.hipHccModuleLaunchKernel.startEvent <<
"," 2292 <<
" stopEvent=" << data->args.hipHccModuleLaunchKernel.stopEvent
2295 case HIP_API_ID_hipFree:
2297 <<
" ptr=" << data->args.hipFree.ptr
2300 case HIP_API_ID_hipDeviceGetAttribute:
2301 oss <<
"hipDeviceGetAttribute(" 2302 <<
" pi=" << data->args.hipDeviceGetAttribute.pi <<
"," 2303 <<
" attr=" << data->args.hipDeviceGetAttribute.attr <<
"," 2304 <<
" deviceId=" << data->args.hipDeviceGetAttribute.deviceId
2307 case HIP_API_ID_hipMemcpyDtoH:
2308 oss <<
"hipMemcpyDtoH(" 2309 <<
" dst=" << data->args.hipMemcpyDtoH.dst <<
"," 2310 <<
" src=" << data->args.hipMemcpyDtoH.src <<
"," 2311 <<
" sizeBytes=" << data->args.hipMemcpyDtoH.sizeBytes
2314 case HIP_API_ID_hipCtxDisablePeerAccess:
2315 oss <<
"hipCtxDisablePeerAccess(" 2316 <<
" peerCtx=" << data->args.hipCtxDisablePeerAccess.peerCtx
2319 case HIP_API_ID_hipDeviceGetByPCIBusId:
2320 oss <<
"hipDeviceGetByPCIBusId(" 2321 <<
" device=" << data->args.hipDeviceGetByPCIBusId.device <<
"," 2322 <<
" pciBusId=" << data->args.hipDeviceGetByPCIBusId.pciBusId
2325 case HIP_API_ID_hipIpcGetMemHandle:
2326 oss <<
"hipIpcGetMemHandle(" 2327 <<
" handle=" << data->args.hipIpcGetMemHandle.handle <<
"," 2328 <<
" devPtr=" << data->args.hipIpcGetMemHandle.devPtr
2331 case HIP_API_ID_hipMemcpyHtoDAsync:
2332 oss <<
"hipMemcpyHtoDAsync(" 2333 <<
" dst=" << data->args.hipMemcpyHtoDAsync.dst <<
"," 2334 <<
" src=" << data->args.hipMemcpyHtoDAsync.src <<
"," 2335 <<
" sizeBytes=" << data->args.hipMemcpyHtoDAsync.sizeBytes <<
"," 2336 <<
" stream=" << data->args.hipMemcpyHtoDAsync.stream
2339 case HIP_API_ID_hipCtxGetDevice:
2340 oss <<
"hipCtxGetDevice(" 2341 <<
" device=" << data->args.hipCtxGetDevice.device
2344 case HIP_API_ID_hipMemset3D:
2345 oss <<
"hipMemset3D(" 2346 <<
" pitchedDevPtr=" << data->args.hipMemset3D.pitchedDevPtr <<
"," 2347 <<
" value=" << data->args.hipMemset3D.value <<
"," 2348 <<
" extent=" << data->args.hipMemset3D.extent
2351 case HIP_API_ID_hipModuleLoadData:
2352 oss <<
"hipModuleLoadData(" 2353 <<
" module=" << data->args.hipModuleLoadData.module <<
"," 2354 <<
" image=" << data->args.hipModuleLoadData.image
2357 case HIP_API_ID_hipDeviceTotalMem:
2358 oss <<
"hipDeviceTotalMem(" 2359 <<
" bytes=" << data->args.hipDeviceTotalMem.bytes <<
"," 2360 <<
" device=" << data->args.hipDeviceTotalMem.device
2363 case HIP_API_ID_hipCtxSetCurrent:
2364 oss <<
"hipCtxSetCurrent(" 2365 <<
" ctx=" << data->args.hipCtxSetCurrent.ctx
2368 case HIP_API_ID_hipGetErrorString:
2369 oss <<
"hipGetErrorString(" 2370 <<
" hipError=" << data->args.hipGetErrorString.hipError
2373 case HIP_API_ID_hipDevicePrimaryCtxRetain:
2374 oss <<
"hipDevicePrimaryCtxRetain(" 2375 <<
" pctx=" << data->args.hipDevicePrimaryCtxRetain.pctx <<
"," 2376 <<
" dev=" << data->args.hipDevicePrimaryCtxRetain.dev
2379 case HIP_API_ID_hipDeviceDisablePeerAccess:
2380 oss <<
"hipDeviceDisablePeerAccess(" 2381 <<
" peerDeviceId=" << data->args.hipDeviceDisablePeerAccess.peerDeviceId
2384 case HIP_API_ID_hipStreamCreateWithFlags:
2385 oss <<
"hipStreamCreateWithFlags(" 2386 <<
" stream=" << data->args.hipStreamCreateWithFlags.stream <<
"," 2387 <<
" flags=" << data->args.hipStreamCreateWithFlags.flags
2390 case HIP_API_ID_hipMemcpyFromArray:
2391 oss <<
"hipMemcpyFromArray(" 2392 <<
" dst=" << data->args.hipMemcpyFromArray.dst <<
"," 2393 <<
" srcArray=" << data->args.hipMemcpyFromArray.srcArray <<
"," 2394 <<
" wOffset=" << data->args.hipMemcpyFromArray.wOffset <<
"," 2395 <<
" hOffset=" << data->args.hipMemcpyFromArray.hOffset <<
"," 2396 <<
" count=" << data->args.hipMemcpyFromArray.count <<
"," 2397 <<
" kind=" << data->args.hipMemcpyFromArray.kind
2400 case HIP_API_ID_hipMemcpy2DAsync:
2401 oss <<
"hipMemcpy2DAsync(" 2402 <<
" dst=" << data->args.hipMemcpy2DAsync.dst <<
"," 2403 <<
" dpitch=" << data->args.hipMemcpy2DAsync.dpitch <<
"," 2404 <<
" src=" << data->args.hipMemcpy2DAsync.src <<
"," 2405 <<
" spitch=" << data->args.hipMemcpy2DAsync.spitch <<
"," 2406 <<
" width=" << data->args.hipMemcpy2DAsync.width <<
"," 2407 <<
" height=" << data->args.hipMemcpy2DAsync.height <<
"," 2408 <<
" kind=" << data->args.hipMemcpy2DAsync.kind <<
"," 2409 <<
" stream=" << data->args.hipMemcpy2DAsync.stream
2412 case HIP_API_ID_hipGetSymbolSize:
2413 oss <<
"hipGetSymbolSize(" 2414 <<
" size=" << data->args.hipGetSymbolSize.size <<
"," 2415 <<
" symbolName=" << data->args.hipGetSymbolSize.symbolName
2418 case HIP_API_ID_hipEventCreateWithFlags:
2419 oss <<
"hipEventCreateWithFlags(" 2420 <<
" event=" << data->args.hipEventCreateWithFlags.event <<
"," 2421 <<
" flags=" << data->args.hipEventCreateWithFlags.flags
2424 case HIP_API_ID_hipStreamQuery:
2425 oss <<
"hipStreamQuery(" 2426 <<
" stream=" << data->args.hipStreamQuery.stream
2429 case HIP_API_ID_hipDeviceGetPCIBusId:
2430 oss <<
"hipDeviceGetPCIBusId(" 2431 <<
" pciBusId=" << data->args.hipDeviceGetPCIBusId.pciBusId <<
"," 2432 <<
" len=" << data->args.hipDeviceGetPCIBusId.len <<
"," 2433 <<
" device=" << data->args.hipDeviceGetPCIBusId.device
2436 case HIP_API_ID_hipMemcpy:
2438 <<
" dst=" << data->args.hipMemcpy.dst <<
"," 2439 <<
" src=" << data->args.hipMemcpy.src <<
"," 2440 <<
" sizeBytes=" << data->args.hipMemcpy.sizeBytes <<
"," 2441 <<
" kind=" << data->args.hipMemcpy.kind
2444 case HIP_API_ID_hipPeekAtLastError:
2445 oss <<
"hipPeekAtLastError(" 2448 case HIP_API_ID_hipStreamAddCallback:
2449 oss <<
"hipStreamAddCallback(" 2450 <<
" stream=" << data->args.hipStreamAddCallback.stream <<
"," 2451 <<
" callback=" << data->args.hipStreamAddCallback.callback <<
"," 2452 <<
" userData=" << data->args.hipStreamAddCallback.userData <<
"," 2453 <<
" flags=" << data->args.hipStreamAddCallback.flags
2456 case HIP_API_ID_hipMemcpyToArray:
2457 oss <<
"hipMemcpyToArray(" 2458 <<
" dst=" << data->args.hipMemcpyToArray.dst <<
"," 2459 <<
" wOffset=" << data->args.hipMemcpyToArray.wOffset <<
"," 2460 <<
" hOffset=" << data->args.hipMemcpyToArray.hOffset <<
"," 2461 <<
" src=" << data->args.hipMemcpyToArray.src <<
"," 2462 <<
" count=" << data->args.hipMemcpyToArray.count <<
"," 2463 <<
" kind=" << data->args.hipMemcpyToArray.kind
2466 case HIP_API_ID_hipMemsetD32:
2467 oss <<
"hipMemsetD32(" 2468 <<
" dest=" << data->args.hipMemsetD32.dest <<
"," 2469 <<
" value=" << data->args.hipMemsetD32.value <<
"," 2470 <<
" count=" << data->args.hipMemsetD32.count
2473 case HIP_API_ID_hipDeviceSynchronize:
2474 oss <<
"hipDeviceSynchronize(" 2477 case HIP_API_ID_hipDeviceGetCacheConfig:
2478 oss <<
"hipDeviceGetCacheConfig(" 2479 <<
" cacheConfig=" << data->args.hipDeviceGetCacheConfig.cacheConfig
2482 case HIP_API_ID_hipMalloc3D:
2483 oss <<
"hipMalloc3D(" 2484 <<
" pitchedDevPtr=" << data->args.hipMalloc3D.pitchedDevPtr <<
"," 2485 <<
" extent=" << data->args.hipMalloc3D.extent
2488 case HIP_API_ID_hipPointerGetAttributes:
2489 oss <<
"hipPointerGetAttributes(" 2490 <<
" attributes=" << data->args.hipPointerGetAttributes.attributes <<
"," 2491 <<
" ptr=" << data->args.hipPointerGetAttributes.ptr
2494 case HIP_API_ID_hipMemsetAsync:
2495 oss <<
"hipMemsetAsync(" 2496 <<
" dst=" << data->args.hipMemsetAsync.dst <<
"," 2497 <<
" value=" << data->args.hipMemsetAsync.value <<
"," 2498 <<
" sizeBytes=" << data->args.hipMemsetAsync.sizeBytes <<
"," 2499 <<
" stream=" << data->args.hipMemsetAsync.stream
2502 case HIP_API_ID_hipMemcpyToSymbol:
2503 oss <<
"hipMemcpyToSymbol(" 2504 <<
" symbolName=" << data->args.hipMemcpyToSymbol.symbolName <<
"," 2505 <<
" src=" << data->args.hipMemcpyToSymbol.src <<
"," 2506 <<
" sizeBytes=" << data->args.hipMemcpyToSymbol.sizeBytes <<
"," 2507 <<
" offset=" << data->args.hipMemcpyToSymbol.offset <<
"," 2508 <<
" kind=" << data->args.hipMemcpyToSymbol.kind
2511 case HIP_API_ID_hipCtxPushCurrent:
2512 oss <<
"hipCtxPushCurrent(" 2513 <<
" ctx=" << data->args.hipCtxPushCurrent.ctx
2516 case HIP_API_ID_hipMemcpyPeer:
2517 oss <<
"hipMemcpyPeer(" 2518 <<
" dst=" << data->args.hipMemcpyPeer.dst <<
"," 2519 <<
" dstDeviceId=" << data->args.hipMemcpyPeer.dstDeviceId <<
"," 2520 <<
" src=" << data->args.hipMemcpyPeer.src <<
"," 2521 <<
" srcDeviceId=" << data->args.hipMemcpyPeer.srcDeviceId <<
"," 2522 <<
" sizeBytes=" << data->args.hipMemcpyPeer.sizeBytes
2525 case HIP_API_ID_hipEventSynchronize:
2526 oss <<
"hipEventSynchronize(" 2527 <<
" event=" << data->args.hipEventSynchronize.event
2530 case HIP_API_ID_hipMemcpyDtoDAsync:
2531 oss <<
"hipMemcpyDtoDAsync(" 2532 <<
" dst=" << data->args.hipMemcpyDtoDAsync.dst <<
"," 2533 <<
" src=" << data->args.hipMemcpyDtoDAsync.src <<
"," 2534 <<
" sizeBytes=" << data->args.hipMemcpyDtoDAsync.sizeBytes <<
"," 2535 <<
" stream=" << data->args.hipMemcpyDtoDAsync.stream
2538 case HIP_API_ID_hipExtMallocWithFlags:
2539 oss <<
"hipExtMallocWithFlags(" 2540 <<
" ptr=" << data->args.hipExtMallocWithFlags.ptr <<
"," 2541 <<
" sizeBytes=" << data->args.hipExtMallocWithFlags.sizeBytes <<
"," 2542 <<
" flags=" << data->args.hipExtMallocWithFlags.flags
2545 case HIP_API_ID_hipCtxEnablePeerAccess:
2546 oss <<
"hipCtxEnablePeerAccess(" 2547 <<
" peerCtx=" << data->args.hipCtxEnablePeerAccess.peerCtx <<
"," 2548 <<
" flags=" << data->args.hipCtxEnablePeerAccess.flags
2551 case HIP_API_ID_hipMemcpyDtoHAsync:
2552 oss <<
"hipMemcpyDtoHAsync(" 2553 <<
" dst=" << data->args.hipMemcpyDtoHAsync.dst <<
"," 2554 <<
" src=" << data->args.hipMemcpyDtoHAsync.src <<
"," 2555 <<
" sizeBytes=" << data->args.hipMemcpyDtoHAsync.sizeBytes <<
"," 2556 <<
" stream=" << data->args.hipMemcpyDtoHAsync.stream
2559 case HIP_API_ID_hipModuleLaunchKernel:
2560 oss <<
"hipModuleLaunchKernel(" 2561 <<
" f=" << data->args.hipModuleLaunchKernel.f <<
"," 2562 <<
" gridDimX=" << data->args.hipModuleLaunchKernel.gridDimX <<
"," 2563 <<
" gridDimY=" << data->args.hipModuleLaunchKernel.gridDimY <<
"," 2564 <<
" gridDimZ=" << data->args.hipModuleLaunchKernel.gridDimZ <<
"," 2565 <<
" blockDimX=" << data->args.hipModuleLaunchKernel.blockDimX <<
"," 2566 <<
" blockDimY=" << data->args.hipModuleLaunchKernel.blockDimY <<
"," 2567 <<
" blockDimZ=" << data->args.hipModuleLaunchKernel.blockDimZ <<
"," 2568 <<
" sharedMemBytes=" << data->args.hipModuleLaunchKernel.sharedMemBytes <<
"," 2569 <<
" stream=" << data->args.hipModuleLaunchKernel.stream <<
"," 2570 <<
" kernelParams=" << data->args.hipModuleLaunchKernel.kernelParams <<
"," 2571 <<
" extra=" << data->args.hipModuleLaunchKernel.extra
2574 case HIP_API_ID_hipModuleGetTexRef:
2575 oss <<
"hipModuleGetTexRef(" 2576 <<
" texRef=" << data->args.hipModuleGetTexRef.texRef <<
"," 2577 <<
" hmod=" << data->args.hipModuleGetTexRef.hmod <<
"," 2578 <<
" name=" << data->args.hipModuleGetTexRef.name
2581 case HIP_API_ID_hipDeviceGetLimit:
2582 oss <<
"hipDeviceGetLimit(" 2583 <<
" pValue=" << data->args.hipDeviceGetLimit.pValue <<
"," 2584 <<
" limit=" << data->args.hipDeviceGetLimit.limit
2587 case HIP_API_ID_hipModuleLoadDataEx:
2588 oss <<
"hipModuleLoadDataEx(" 2589 <<
" module=" << data->args.hipModuleLoadDataEx.module <<
"," 2590 <<
" image=" << data->args.hipModuleLoadDataEx.image <<
"," 2591 <<
" numOptions=" << data->args.hipModuleLoadDataEx.numOptions <<
"," 2592 <<
" options=" << data->args.hipModuleLoadDataEx.options <<
"," 2593 <<
" optionValues=" << data->args.hipModuleLoadDataEx.optionValues
2596 case HIP_API_ID_hipRuntimeGetVersion:
2597 oss <<
"hipRuntimeGetVersion(" 2598 <<
" runtimeVersion=" << data->args.hipRuntimeGetVersion.runtimeVersion
2601 case HIP_API_ID_hipGetDeviceProperties:
2602 oss <<
"hipGetDeviceProperties(" 2603 <<
" prop=" << data->args.hipGetDeviceProperties.prop <<
"," 2604 <<
" deviceId=" << data->args.hipGetDeviceProperties.deviceId
2607 case HIP_API_ID_hipFreeArray:
2608 oss <<
"hipFreeArray(" 2609 <<
" array=" << data->args.hipFreeArray.array
2612 case HIP_API_ID_hipDevicePrimaryCtxRelease:
2613 oss <<
"hipDevicePrimaryCtxRelease(" 2614 <<
" dev=" << data->args.hipDevicePrimaryCtxRelease.dev
2617 case HIP_API_ID_hipHostGetDevicePointer:
2618 oss <<
"hipHostGetDevicePointer(" 2619 <<
" devPtr=" << data->args.hipHostGetDevicePointer.devPtr <<
"," 2620 <<
" hstPtr=" << data->args.hipHostGetDevicePointer.hstPtr <<
"," 2621 <<
" flags=" << data->args.hipHostGetDevicePointer.flags
2624 case HIP_API_ID_hipMemcpyParam2D:
2625 oss <<
"hipMemcpyParam2D(" 2626 <<
" pCopy=" << data->args.hipMemcpyParam2D.pCopy
2629 case HIP_API_ID_hipModuleGetFunction:
2630 oss <<
"hipModuleGetFunction(" 2631 <<
" function=" << data->args.hipModuleGetFunction.function <<
"," 2632 <<
" module=" << data->args.hipModuleGetFunction.module <<
"," 2633 <<
" kname=" << data->args.hipModuleGetFunction.kname
2636 case HIP_API_ID_hipMemsetD32Async:
2637 oss <<
"hipMemsetD32Async(" 2638 <<
" dst=" << data->args.hipMemsetD32Async.dst <<
"," 2639 <<
" value=" << data->args.hipMemsetD32Async.value <<
"," 2640 <<
" count=" << data->args.hipMemsetD32Async.count <<
"," 2641 <<
" stream=" << data->args.hipMemsetD32Async.stream
2644 case HIP_API_ID_hipGetDevice:
2645 oss <<
"hipGetDevice(" 2646 <<
" deviceId=" << data->args.hipGetDevice.deviceId
2649 case HIP_API_ID_hipGetDeviceCount:
2650 oss <<
"hipGetDeviceCount(" 2651 <<
" count=" << data->args.hipGetDeviceCount.count
2654 default: oss <<
"unknown";
2656 return strdup(oss.str().c_str());
2659 #endif // _HIP_PROF_STR_H Definition: driver_types.h:232
Definition: hip_runtime_api.h:137
Definition: hip_module.cpp:89
Definition: hip_hcc_internal.h:880
Definition: texture_types.h:73
Definition: driver_types.h:70
hipDeviceAttribute_t
Definition: hip_runtime_api.h:259
void(* hipStreamCallback_t)(hipStream_t stream, hipError_t status, void *userData)
Definition: hip_runtime_api.h:816
Definition: driver_types.h:245
Definition: driver_types.h:61
Definition: driver_types.h:225
hipFuncCache_t
Definition: hip_runtime_api.h:241
Definition: hip_runtime_api.h:83
hipSharedMemConfig
Definition: hip_runtime_api.h:252
Definition: hip_hcc_internal.h:700
Definition: hip_hcc_internal.h:519
Definition: driver_types.h:82
Definition: hip_runtime_api.h:105
Definition: hip_hcc_internal.h:367
Definition: hip_prof_str.h:358