codekingpro/portable-devtools
114k
1// This file is generated. Any changes you make will be lost during the next clean build.
2
3// CUDA public interface, for type definitions and api function prototypes
4#include "cuda_runtime_api.h"
5
6// *************************************************************************
7// Definitions of structs to hold parameters for each function
8// *************************************************************************
9
10// Currently used parameter trace structures
11typedef struct cudaDeviceSetLimit_v3020_params_st {
12 enum cudaLimit limit;
13 size_t value;
14} cudaDeviceSetLimit_v3020_params;
15
16typedef struct cudaDeviceGetLimit_v3020_params_st {
17 size_t *pValue;
18 enum cudaLimit limit;
19} cudaDeviceGetLimit_v3020_params;
20
21typedef struct cudaDeviceGetTexture1DLinearMaxWidth_v11010_params_st {
22 size_t *maxWidthInElements;
23 const struct cudaChannelFormatDesc *fmtDesc;
24 int device;
25} cudaDeviceGetTexture1DLinearMaxWidth_v11010_params;
26
27typedef struct cudaDeviceGetCacheConfig_v3020_params_st {
28 enum cudaFuncCache *pCacheConfig;
29} cudaDeviceGetCacheConfig_v3020_params;
30
31typedef struct cudaDeviceGetStreamPriorityRange_v5050_params_st {
32 int *leastPriority;
33 int *greatestPriority;
34} cudaDeviceGetStreamPriorityRange_v5050_params;
35
36typedef struct cudaDeviceSetCacheConfig_v3020_params_st {
37 enum cudaFuncCache cacheConfig;
38} cudaDeviceSetCacheConfig_v3020_params;
39
40typedef struct cudaDeviceGetSharedMemConfig_v4020_params_st {
41 enum cudaSharedMemConfig *pConfig;
42} cudaDeviceGetSharedMemConfig_v4020_params;
43
44typedef struct cudaDeviceSetSharedMemConfig_v4020_params_st {
45 enum cudaSharedMemConfig config;
46} cudaDeviceSetSharedMemConfig_v4020_params;
47
48typedef struct cudaDeviceGetByPCIBusId_v4010_params_st {
49 int *device;
50 const char *pciBusId;
51} cudaDeviceGetByPCIBusId_v4010_params;
52
53typedef struct cudaDeviceGetPCIBusId_v4010_params_st {
54 char *pciBusId;
55 int len;
56 int device;
57} cudaDeviceGetPCIBusId_v4010_params;
58
59typedef struct cudaIpcGetEventHandle_v4010_params_st {
60 cudaIpcEventHandle_t *handle;
61 cudaEvent_t event;
62} cudaIpcGetEventHandle_v4010_params;
63
64typedef struct cudaIpcOpenEventHandle_v4010_params_st {
65 cudaEvent_t *event;
66 cudaIpcEventHandle_t handle;
67} cudaIpcOpenEventHandle_v4010_params;
68
69typedef struct cudaIpcGetMemHandle_v4010_params_st {
70 cudaIpcMemHandle_t *handle;
71 void *devPtr;
72} cudaIpcGetMemHandle_v4010_params;
73
74typedef struct cudaIpcOpenMemHandle_v4010_params_st {
75 void **devPtr;
76 cudaIpcMemHandle_t handle;
77 unsigned int flags;
78} cudaIpcOpenMemHandle_v4010_params;
79
80typedef struct cudaIpcCloseMemHandle_v4010_params_st {
81 void *devPtr;
82} cudaIpcCloseMemHandle_v4010_params;
83
84typedef struct cudaDeviceFlushGPUDirectRDMAWrites_v11030_params_st {
85 enum cudaFlushGPUDirectRDMAWritesTarget target;
86 enum cudaFlushGPUDirectRDMAWritesScope scope;
87} cudaDeviceFlushGPUDirectRDMAWrites_v11030_params;
88
89typedef struct cudaThreadSetLimit_v3020_params_st {
90 enum cudaLimit limit;
91 size_t value;
92} cudaThreadSetLimit_v3020_params;
93
94typedef struct cudaThreadGetLimit_v3020_params_st {
95 size_t *pValue;
96 enum cudaLimit limit;
97} cudaThreadGetLimit_v3020_params;
98
99typedef struct cudaThreadGetCacheConfig_v3020_params_st {
100 enum cudaFuncCache *pCacheConfig;
101} cudaThreadGetCacheConfig_v3020_params;
102
103typedef struct cudaThreadSetCacheConfig_v3020_params_st {
104 enum cudaFuncCache cacheConfig;
105} cudaThreadSetCacheConfig_v3020_params;
106
107typedef struct cudaGetErrorName_v6050_params_st {
108 cudaError_t error;
109} cudaGetErrorName_v6050_params;
110
111typedef struct cudaGetErrorString_v3020_params_st {
112 cudaError_t error;
113} cudaGetErrorString_v3020_params;
114
115typedef struct cudaGetDeviceCount_v3020_params_st {
116 int *count;
117} cudaGetDeviceCount_v3020_params;
118
119typedef struct cudaGetDeviceProperties_v3020_params_st {
120 struct cudaDeviceProp *prop;
121 int device;
122} cudaGetDeviceProperties_v3020_params;
123
124typedef struct cudaDeviceGetAttribute_v5000_params_st {
125 int *value;
126 enum cudaDeviceAttr attr;
127 int device;
128} cudaDeviceGetAttribute_v5000_params;
129
130typedef struct cudaDeviceGetDefaultMemPool_v11020_params_st {
131 cudaMemPool_t *memPool;
132 int device;
133} cudaDeviceGetDefaultMemPool_v11020_params;
134
135typedef struct cudaDeviceSetMemPool_v11020_params_st {
136 int device;
137 cudaMemPool_t memPool;
138} cudaDeviceSetMemPool_v11020_params;
139
140typedef struct cudaDeviceGetMemPool_v11020_params_st {
141 cudaMemPool_t *memPool;
142 int device;
143} cudaDeviceGetMemPool_v11020_params;
144
145typedef struct cudaDeviceGetNvSciSyncAttributes_v10020_params_st {
146 void *nvSciSyncAttrList;
147 int device;
148 int flags;
149} cudaDeviceGetNvSciSyncAttributes_v10020_params;
150
151typedef struct cudaDeviceGetP2PAttribute_v8000_params_st {
152 int *value;
153 enum cudaDeviceP2PAttr attr;
154 int srcDevice;
155 int dstDevice;
156} cudaDeviceGetP2PAttribute_v8000_params;
157
158typedef struct cudaChooseDevice_v3020_params_st {
159 int *device;
160 const struct cudaDeviceProp *prop;
161} cudaChooseDevice_v3020_params;
162
163typedef struct cudaSetDevice_v3020_params_st {
164 int device;
165} cudaSetDevice_v3020_params;
166
167typedef struct cudaGetDevice_v3020_params_st {
168 int *device;
169} cudaGetDevice_v3020_params;
170
171typedef struct cudaSetValidDevices_v3020_params_st {
172 int *device_arr;
173 int len;
174} cudaSetValidDevices_v3020_params;
175
176typedef struct cudaSetDeviceFlags_v3020_params_st {
177 unsigned int flags;
178} cudaSetDeviceFlags_v3020_params;
179
180typedef struct cudaGetDeviceFlags_v7000_params_st {
181 unsigned int *flags;
182} cudaGetDeviceFlags_v7000_params;
183
184typedef struct cudaStreamCreate_v3020_params_st {
185 cudaStream_t *pStream;
186} cudaStreamCreate_v3020_params;
187
188typedef struct cudaStreamCreateWithFlags_v5000_params_st {
189 cudaStream_t *pStream;
190 unsigned int flags;
191} cudaStreamCreateWithFlags_v5000_params;
192
193typedef struct cudaStreamCreateWithPriority_v5050_params_st {
194 cudaStream_t *pStream;
195 unsigned int flags;
196 int priority;
197} cudaStreamCreateWithPriority_v5050_params;
198
199typedef struct cudaStreamGetPriority_ptsz_v7000_params_st {
200 cudaStream_t hStream;
201 int *priority;
202} cudaStreamGetPriority_ptsz_v7000_params;
203
204typedef struct cudaStreamGetFlags_ptsz_v7000_params_st {
205 cudaStream_t hStream;
206 unsigned int *flags;
207} cudaStreamGetFlags_ptsz_v7000_params;
208
209typedef struct cudaStreamGetId_ptsz_v12000_params_st {
210 cudaStream_t hStream;
211 unsigned long long *streamId;
212} cudaStreamGetId_ptsz_v12000_params;
213
214typedef struct cudaStreamCopyAttributes_ptsz_v11000_params_st {
215 cudaStream_t dst;
216 cudaStream_t src;
217} cudaStreamCopyAttributes_ptsz_v11000_params;
218
219typedef struct cudaStreamGetAttribute_ptsz_v11000_params_st {
220 cudaStream_t hStream;
221 cudaStreamAttrID attr;
222 cudaStreamAttrValue *value_out;
223} cudaStreamGetAttribute_ptsz_v11000_params;
224
225typedef struct cudaStreamSetAttribute_ptsz_v11000_params_st {
226 cudaStream_t hStream;
227 cudaStreamAttrID attr;
228 const cudaStreamAttrValue *value;
229} cudaStreamSetAttribute_ptsz_v11000_params;
230
231typedef struct cudaStreamDestroy_v5050_params_st {
232 cudaStream_t stream;
233} cudaStreamDestroy_v5050_params;
234
235typedef struct cudaStreamWaitEvent_ptsz_v7000_params_st {
236 cudaStream_t stream;
237 cudaEvent_t event;
238 unsigned int flags;
239} cudaStreamWaitEvent_ptsz_v7000_params;
240
241typedef struct cudaStreamAddCallback_ptsz_v7000_params_st {
242 cudaStream_t stream;
243 cudaStreamCallback_t callback;
244 void *userData;
245 unsigned int flags;
246} cudaStreamAddCallback_ptsz_v7000_params;
247
248typedef struct cudaStreamSynchronize_ptsz_v7000_params_st {
249 cudaStream_t stream;
250} cudaStreamSynchronize_ptsz_v7000_params;
251
252typedef struct cudaStreamQuery_ptsz_v7000_params_st {
253 cudaStream_t stream;
254} cudaStreamQuery_ptsz_v7000_params;
255
256typedef struct cudaStreamAttachMemAsync_ptsz_v7000_params_st {
257 cudaStream_t stream;
258 void *devPtr;
259 size_t length;
260 unsigned int flags;
261} cudaStreamAttachMemAsync_ptsz_v7000_params;
262
263typedef struct cudaStreamBeginCapture_ptsz_v10000_params_st {
264 cudaStream_t stream;
265 enum cudaStreamCaptureMode mode;
266} cudaStreamBeginCapture_ptsz_v10000_params;
267
268typedef struct cudaThreadExchangeStreamCaptureMode_v10010_params_st {
269 enum cudaStreamCaptureMode *mode;
270} cudaThreadExchangeStreamCaptureMode_v10010_params;
271
272typedef struct cudaStreamEndCapture_ptsz_v10000_params_st {
273 cudaStream_t stream;
274 cudaGraph_t *pGraph;
275} cudaStreamEndCapture_ptsz_v10000_params;
276
277typedef struct cudaStreamIsCapturing_ptsz_v10000_params_st {
278 cudaStream_t stream;
279 enum cudaStreamCaptureStatus *pCaptureStatus;
280} cudaStreamIsCapturing_ptsz_v10000_params;
281
282typedef struct cudaStreamGetCaptureInfo_ptsz_v10010_params_st {
283 cudaStream_t stream;
284 enum cudaStreamCaptureStatus *pCaptureStatus;
285 unsigned long long *pId;
286} cudaStreamGetCaptureInfo_ptsz_v10010_params;
287
288typedef struct cudaStreamGetCaptureInfo_v2_ptsz_v11030_params_st {
289 cudaStream_t stream;
290 enum cudaStreamCaptureStatus *captureStatus_out;
291 unsigned long long *id_out;
292 cudaGraph_t *graph_out;
293 const cudaGraphNode_t **dependencies_out;
294 size_t *numDependencies_out;
295} cudaStreamGetCaptureInfo_v2_ptsz_v11030_params;
296
297typedef struct cudaStreamUpdateCaptureDependencies_ptsz_v11030_params_st {
298 cudaStream_t stream;
299 cudaGraphNode_t *dependencies;
300 size_t numDependencies;
301 unsigned int flags;
302} cudaStreamUpdateCaptureDependencies_ptsz_v11030_params;
303
304typedef struct cudaEventCreate_v3020_params_st {
305 cudaEvent_t *event;
306} cudaEventCreate_v3020_params;
307
308typedef struct cudaEventCreateWithFlags_v3020_params_st {
309 cudaEvent_t *event;
310 unsigned int flags;
311} cudaEventCreateWithFlags_v3020_params;
312
313typedef struct cudaEventRecord_ptsz_v7000_params_st {
314 cudaEvent_t event;
315 cudaStream_t stream;
316} cudaEventRecord_ptsz_v7000_params;
317
318typedef struct cudaEventRecordWithFlags_ptsz_v11010_params_st {
319 cudaEvent_t event;
320 cudaStream_t stream;
321 unsigned int flags;
322} cudaEventRecordWithFlags_ptsz_v11010_params;
323
324typedef struct cudaEventQuery_v3020_params_st {
325 cudaEvent_t event;
326} cudaEventQuery_v3020_params;
327
328typedef struct cudaEventSynchronize_v3020_params_st {
329 cudaEvent_t event;
330} cudaEventSynchronize_v3020_params;
331
332typedef struct cudaEventDestroy_v3020_params_st {
333 cudaEvent_t event;
334} cudaEventDestroy_v3020_params;
335
336typedef struct cudaEventElapsedTime_v3020_params_st {
337 float *ms;
338 cudaEvent_t start;
339 cudaEvent_t end;
340} cudaEventElapsedTime_v3020_params;
341
342typedef struct cudaImportExternalMemory_v10000_params_st {
343 cudaExternalMemory_t *extMem_out;
344 const struct cudaExternalMemoryHandleDesc *memHandleDesc;
345} cudaImportExternalMemory_v10000_params;
346
347typedef struct cudaExternalMemoryGetMappedBuffer_v10000_params_st {
348 void **devPtr;
349 cudaExternalMemory_t extMem;
350 const struct cudaExternalMemoryBufferDesc *bufferDesc;
351} cudaExternalMemoryGetMappedBuffer_v10000_params;
352
353typedef struct cudaExternalMemoryGetMappedMipmappedArray_v10000_params_st {
354 cudaMipmappedArray_t *mipmap;
355 cudaExternalMemory_t extMem;
356 const struct cudaExternalMemoryMipmappedArrayDesc *mipmapDesc;
357} cudaExternalMemoryGetMappedMipmappedArray_v10000_params;
358
359typedef struct cudaDestroyExternalMemory_v10000_params_st {
360 cudaExternalMemory_t extMem;
361} cudaDestroyExternalMemory_v10000_params;
362
363typedef struct cudaImportExternalSemaphore_v10000_params_st {
364 cudaExternalSemaphore_t *extSem_out;
365 const struct cudaExternalSemaphoreHandleDesc *semHandleDesc;
366} cudaImportExternalSemaphore_v10000_params;
367
368typedef struct cudaSignalExternalSemaphoresAsync_v2_ptsz_v11020_params_st {
369 const cudaExternalSemaphore_t *extSemArray;
370 const struct cudaExternalSemaphoreSignalParams *paramsArray;
371 unsigned int numExtSems;
372 cudaStream_t stream;
373} cudaSignalExternalSemaphoresAsync_v2_ptsz_v11020_params;
374
375typedef struct cudaWaitExternalSemaphoresAsync_v2_ptsz_v11020_params_st {
376 const cudaExternalSemaphore_t *extSemArray;
377 const struct cudaExternalSemaphoreWaitParams *paramsArray;
378 unsigned int numExtSems;
379 cudaStream_t stream;
380} cudaWaitExternalSemaphoresAsync_v2_ptsz_v11020_params;
381
382typedef struct cudaDestroyExternalSemaphore_v10000_params_st {
383 cudaExternalSemaphore_t extSem;
384} cudaDestroyExternalSemaphore_v10000_params;
385
386typedef struct cudaLaunchKernel_ptsz_v7000_params_st {
387 const void *func;
388 dim3 gridDim;
389 dim3 blockDim;
390 void **args;
391 size_t sharedMem;
392 cudaStream_t stream;
393} cudaLaunchKernel_ptsz_v7000_params;
394
395typedef struct cudaLaunchKernelExC_ptsz_v11060_params_st {
396 const cudaLaunchConfig_t *config;
397 const void *func;
398 void **args;
399} cudaLaunchKernelExC_ptsz_v11060_params;
400
401typedef struct cudaLaunchCooperativeKernel_ptsz_v9000_params_st {
402 const void *func;
403 dim3 gridDim;
404 dim3 blockDim;
405 void **args;
406 size_t sharedMem;
407 cudaStream_t stream;
408} cudaLaunchCooperativeKernel_ptsz_v9000_params;
409
410typedef struct cudaLaunchCooperativeKernelMultiDevice_v9000_params_st {
411 struct cudaLaunchParams *launchParamsList;
412 unsigned int numDevices;
413 unsigned int flags;
414} cudaLaunchCooperativeKernelMultiDevice_v9000_params;
415
416typedef struct cudaFuncSetCacheConfig_v3020_params_st {
417 const void *func;
418 enum cudaFuncCache cacheConfig;
419} cudaFuncSetCacheConfig_v3020_params;
420
421typedef struct cudaFuncSetSharedMemConfig_v4020_params_st {
422 const void *func;
423 enum cudaSharedMemConfig config;
424} cudaFuncSetSharedMemConfig_v4020_params;
425
426typedef struct cudaFuncGetAttributes_v3020_params_st {
427 struct cudaFuncAttributes *attr;
428 const void *func;
429} cudaFuncGetAttributes_v3020_params;
430
431typedef struct cudaFuncSetAttribute_v9000_params_st {
432 const void *func;
433 enum cudaFuncAttribute attr;
434 int value;
435} cudaFuncSetAttribute_v9000_params;
436
437typedef struct cudaSetDoubleForDevice_v3020_params_st {
438 double *d;
439} cudaSetDoubleForDevice_v3020_params;
440
441typedef struct cudaSetDoubleForHost_v3020_params_st {
442 double *d;
443} cudaSetDoubleForHost_v3020_params;
444
445typedef struct cudaLaunchHostFunc_ptsz_v10000_params_st {
446 cudaStream_t stream;
447 cudaHostFn_t fn;
448 void *userData;
449} cudaLaunchHostFunc_ptsz_v10000_params;
450
451typedef struct cudaOccupancyMaxActiveBlocksPerMultiprocessor_v6050_params_st {
452 int *numBlocks;
453 const void *func;
454 int blockSize;
455 size_t dynamicSMemSize;
456} cudaOccupancyMaxActiveBlocksPerMultiprocessor_v6050_params;
457
458typedef struct cudaOccupancyAvailableDynamicSMemPerBlock_v10200_params_st {
459 size_t *dynamicSmemSize;
460 const void *func;
461 int numBlocks;
462 int blockSize;
463} cudaOccupancyAvailableDynamicSMemPerBlock_v10200_params;
464
465typedef struct cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags_v7000_params_st {
466 int *numBlocks;
467 const void *func;
468 int blockSize;
469 size_t dynamicSMemSize;
470 unsigned int flags;
471} cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags_v7000_params;
472
473typedef struct cudaOccupancyMaxPotentialClusterSize_v11070_params_st {
474 int *clusterSize;
475 const void *func;
476 const cudaLaunchConfig_t *launchConfig;
477} cudaOccupancyMaxPotentialClusterSize_v11070_params;
478
479typedef struct cudaOccupancyMaxActiveClusters_v11070_params_st {
480 int *numClusters;
481 const void *func;
482 const cudaLaunchConfig_t *launchConfig;
483} cudaOccupancyMaxActiveClusters_v11070_params;
484
485typedef struct cudaMallocManaged_v6000_params_st {
486 void **devPtr;
487 size_t size;
488 unsigned int flags;
489} cudaMallocManaged_v6000_params;
490
491typedef struct cudaMalloc_v3020_params_st {
492 void **devPtr;
493 size_t size;
494} cudaMalloc_v3020_params;
495
496typedef struct cudaMallocHost_v3020_params_st {
497 void **ptr;
498 size_t size;
499} cudaMallocHost_v3020_params;
500
501typedef struct cudaMallocPitch_v3020_params_st {
502 void **devPtr;
503 size_t *pitch;
504 size_t width;
505 size_t height;
506} cudaMallocPitch_v3020_params;
507
508typedef struct cudaMallocArray_v3020_params_st {
509 cudaArray_t *array;
510 const struct cudaChannelFormatDesc *desc;
511 size_t width;
512 size_t height;
513 unsigned int flags;
514} cudaMallocArray_v3020_params;
515
516typedef struct cudaFree_v3020_params_st {
517 void *devPtr;
518} cudaFree_v3020_params;
519
520typedef struct cudaFreeHost_v3020_params_st {
521 void *ptr;
522} cudaFreeHost_v3020_params;
523
524typedef struct cudaFreeArray_v3020_params_st {
525 cudaArray_t array;
526} cudaFreeArray_v3020_params;
527
528typedef struct cudaFreeMipmappedArray_v5000_params_st {
529 cudaMipmappedArray_t mipmappedArray;
530} cudaFreeMipmappedArray_v5000_params;
531
532typedef struct cudaHostAlloc_v3020_params_st {
533 void **pHost;
534 size_t size;
535 unsigned int flags;
536} cudaHostAlloc_v3020_params;
537
538typedef struct cudaHostRegister_v4000_params_st {
539 void *ptr;
540 size_t size;
541 unsigned int flags;
542} cudaHostRegister_v4000_params;
543
544typedef struct cudaHostUnregister_v4000_params_st {
545 void *ptr;
546} cudaHostUnregister_v4000_params;
547
548typedef struct cudaHostGetDevicePointer_v3020_params_st {
549 void **pDevice;
550 void *pHost;
551 unsigned int flags;
552} cudaHostGetDevicePointer_v3020_params;
553
554typedef struct cudaHostGetFlags_v3020_params_st {
555 unsigned int *pFlags;
556 void *pHost;
557} cudaHostGetFlags_v3020_params;
558
559typedef struct cudaMalloc3D_v3020_params_st {
560 struct cudaPitchedPtr *pitchedDevPtr;
561 struct cudaExtent extent;
562} cudaMalloc3D_v3020_params;
563
564typedef struct cudaMalloc3DArray_v3020_params_st {
565 cudaArray_t *array;
566 const struct cudaChannelFormatDesc *desc;
567 struct cudaExtent extent;
568 unsigned int flags;
569} cudaMalloc3DArray_v3020_params;
570
571typedef struct cudaMallocMipmappedArray_v5000_params_st {
572 cudaMipmappedArray_t *mipmappedArray;
573 const struct cudaChannelFormatDesc *desc;
574 struct cudaExtent extent;
575 unsigned int numLevels;
576 unsigned int flags;
577} cudaMallocMipmappedArray_v5000_params;
578
579typedef struct cudaGetMipmappedArrayLevel_v5000_params_st {
580 cudaArray_t *levelArray;
581 cudaMipmappedArray_const_t mipmappedArray;
582 unsigned int level;
583} cudaGetMipmappedArrayLevel_v5000_params;
584
585typedef struct cudaMemcpy3D_ptds_v7000_params_st {
586 const struct cudaMemcpy3DParms *p;
587} cudaMemcpy3D_ptds_v7000_params;
588
589typedef struct cudaMemcpy3DPeer_ptds_v7000_params_st {
590 const struct cudaMemcpy3DPeerParms *p;
591} cudaMemcpy3DPeer_ptds_v7000_params;
592
593typedef struct cudaMemcpy3DAsync_ptsz_v7000_params_st {
594 const struct cudaMemcpy3DParms *p;
595 cudaStream_t stream;
596} cudaMemcpy3DAsync_ptsz_v7000_params;
597
598typedef struct cudaMemcpy3DPeerAsync_ptsz_v7000_params_st {
599 const struct cudaMemcpy3DPeerParms *p;
600 cudaStream_t stream;
601} cudaMemcpy3DPeerAsync_ptsz_v7000_params;
602
603typedef struct cudaMemGetInfo_v3020_params_st {
604 size_t *free;
605 size_t *total;
606} cudaMemGetInfo_v3020_params;
607
608typedef struct cudaArrayGetInfo_v4010_params_st {
609 struct cudaChannelFormatDesc *desc;
610 struct cudaExtent *extent;
611 unsigned int *flags;
612 cudaArray_t array;
613} cudaArrayGetInfo_v4010_params;
614
615typedef struct cudaArrayGetPlane_v11020_params_st {
616 cudaArray_t *pPlaneArray;
617 cudaArray_t hArray;
618 unsigned int planeIdx;
619} cudaArrayGetPlane_v11020_params;
620
621typedef struct cudaArrayGetMemoryRequirements_v11060_params_st {
622 struct cudaArrayMemoryRequirements *memoryRequirements;
623 cudaArray_t array;
624 int device;
625} cudaArrayGetMemoryRequirements_v11060_params;
626
627typedef struct cudaMipmappedArrayGetMemoryRequirements_v11060_params_st {
628 struct cudaArrayMemoryRequirements *memoryRequirements;
629 cudaMipmappedArray_t mipmap;
630 int device;
631} cudaMipmappedArrayGetMemoryRequirements_v11060_params;
632
633typedef struct cudaArrayGetSparseProperties_v11010_params_st {
634 struct cudaArraySparseProperties *sparseProperties;
635 cudaArray_t array;
636} cudaArrayGetSparseProperties_v11010_params;
637
638typedef struct cudaMipmappedArrayGetSparseProperties_v11010_params_st {
639 struct cudaArraySparseProperties *sparseProperties;
640 cudaMipmappedArray_t mipmap;
641} cudaMipmappedArrayGetSparseProperties_v11010_params;
642
643typedef struct cudaMemcpy_ptds_v7000_params_st {
644 void *dst;
645 const void *src;
646 size_t count;
647 enum cudaMemcpyKind kind;
648} cudaMemcpy_ptds_v7000_params;
649
650typedef struct cudaMemcpyPeer_v4000_params_st {
651 void *dst;
652 int dstDevice;
653 const void *src;
654 int srcDevice;
655 size_t count;
656} cudaMemcpyPeer_v4000_params;
657
658typedef struct cudaMemcpy2D_ptds_v7000_params_st {
659 void *dst;
660 size_t dpitch;
661 const void *src;
662 size_t spitch;
663 size_t width;
664 size_t height;
665 enum cudaMemcpyKind kind;
666} cudaMemcpy2D_ptds_v7000_params;
667
668typedef struct cudaMemcpy2DToArray_ptds_v7000_params_st {
669 cudaArray_t dst;
670 size_t wOffset;
671 size_t hOffset;
672 const void *src;
673 size_t spitch;
674 size_t width;
675 size_t height;
676 enum cudaMemcpyKind kind;
677} cudaMemcpy2DToArray_ptds_v7000_params;
678
679typedef struct cudaMemcpy2DFromArray_ptds_v7000_params_st {
680 void *dst;
681 size_t dpitch;
682 cudaArray_const_t src;
683 size_t wOffset;
684 size_t hOffset;
685 size_t width;
686 size_t height;
687 enum cudaMemcpyKind kind;
688} cudaMemcpy2DFromArray_ptds_v7000_params;
689
690typedef struct cudaMemcpy2DArrayToArray_ptds_v7000_params_st {
691 cudaArray_t dst;
692 size_t wOffsetDst;
693 size_t hOffsetDst;
694 cudaArray_const_t src;
695 size_t wOffsetSrc;
696 size_t hOffsetSrc;
697 size_t width;
698 size_t height;
699 enum cudaMemcpyKind kind;
700} cudaMemcpy2DArrayToArray_ptds_v7000_params;
701
702typedef struct cudaMemcpyToSymbol_ptds_v7000_params_st {
703 const void *symbol;
704 const void *src;
705 size_t count;
706 size_t offset;
707 enum cudaMemcpyKind kind;
708} cudaMemcpyToSymbol_ptds_v7000_params;
709
710typedef struct cudaMemcpyFromSymbol_ptds_v7000_params_st {
711 void *dst;
712 const void *symbol;
713 size_t count;
714 size_t offset;
715 enum cudaMemcpyKind kind;
716} cudaMemcpyFromSymbol_ptds_v7000_params;
717
718typedef struct cudaMemcpyAsync_ptsz_v7000_params_st {
719 void *dst;
720 const void *src;
721 size_t count;
722 enum cudaMemcpyKind kind;
723 cudaStream_t stream;
724} cudaMemcpyAsync_ptsz_v7000_params;
725
726typedef struct cudaMemcpyPeerAsync_v4000_params_st {
727 void *dst;
728 int dstDevice;
729 const void *src;
730 int srcDevice;
731 size_t count;
732 cudaStream_t stream;
733} cudaMemcpyPeerAsync_v4000_params;
734
735typedef struct cudaMemcpy2DAsync_ptsz_v7000_params_st {
736 void *dst;
737 size_t dpitch;
738 const void *src;
739 size_t spitch;
740 size_t width;
741 size_t height;
742 enum cudaMemcpyKind kind;
743 cudaStream_t stream;
744} cudaMemcpy2DAsync_ptsz_v7000_params;
745
746typedef struct cudaMemcpy2DToArrayAsync_ptsz_v7000_params_st {
747 cudaArray_t dst;
748 size_t wOffset;
749 size_t hOffset;
750 const void *src;
751 size_t spitch;
752 size_t width;
753 size_t height;
754 enum cudaMemcpyKind kind;
755 cudaStream_t stream;
756} cudaMemcpy2DToArrayAsync_ptsz_v7000_params;
757
758typedef struct cudaMemcpy2DFromArrayAsync_ptsz_v7000_params_st {
759 void *dst;
760 size_t dpitch;
761 cudaArray_const_t src;
762 size_t wOffset;
763 size_t hOffset;
764 size_t width;
765 size_t height;
766 enum cudaMemcpyKind kind;
767 cudaStream_t stream;
768} cudaMemcpy2DFromArrayAsync_ptsz_v7000_params;
769
770typedef struct cudaMemcpyToSymbolAsync_ptsz_v7000_params_st {
771 const void *symbol;
772 const void *src;
773 size_t count;
774 size_t offset;
775 enum cudaMemcpyKind kind;
776 cudaStream_t stream;
777} cudaMemcpyToSymbolAsync_ptsz_v7000_params;
778
779typedef struct cudaMemcpyFromSymbolAsync_ptsz_v7000_params_st {
780 void *dst;
781 const void *symbol;
782 size_t count;
783 size_t offset;
784 enum cudaMemcpyKind kind;
785 cudaStream_t stream;
786} cudaMemcpyFromSymbolAsync_ptsz_v7000_params;
787
788typedef struct cudaMemset_ptds_v7000_params_st {
789 void *devPtr;
790 int value;
791 size_t count;
792} cudaMemset_ptds_v7000_params;
793
794typedef struct cudaMemset2D_ptds_v7000_params_st {
795 void *devPtr;
796 size_t pitch;
797 int value;
798 size_t width;
799 size_t height;
800} cudaMemset2D_ptds_v7000_params;
801
802typedef struct cudaMemset3D_ptds_v7000_params_st {
803 struct cudaPitchedPtr pitchedDevPtr;
804 int value;
805 struct cudaExtent extent;
806} cudaMemset3D_ptds_v7000_params;
807
808typedef struct cudaMemsetAsync_ptsz_v7000_params_st {
809 void *devPtr;
810 int value;
811 size_t count;
812 cudaStream_t stream;
813} cudaMemsetAsync_ptsz_v7000_params;
814
815typedef struct cudaMemset2DAsync_ptsz_v7000_params_st {
816 void *devPtr;
817 size_t pitch;
818 int value;
819 size_t width;
820 size_t height;
821 cudaStream_t stream;
822} cudaMemset2DAsync_ptsz_v7000_params;
823
824typedef struct cudaMemset3DAsync_ptsz_v7000_params_st {
825 struct cudaPitchedPtr pitchedDevPtr;
826 int value;
827 struct cudaExtent extent;
828 cudaStream_t stream;
829} cudaMemset3DAsync_ptsz_v7000_params;
830
831typedef struct cudaGetSymbolAddress_v3020_params_st {
832 void **devPtr;
833 const void *symbol;
834} cudaGetSymbolAddress_v3020_params;
835
836typedef struct cudaGetSymbolSize_v3020_params_st {
837 size_t *size;
838 const void *symbol;
839} cudaGetSymbolSize_v3020_params;
840
841typedef struct cudaMemPrefetchAsync_ptsz_v8000_params_st {
842 const void *devPtr;
843 size_t count;
844 int dstDevice;
845 cudaStream_t stream;
846} cudaMemPrefetchAsync_ptsz_v8000_params;
847
848typedef struct cudaMemAdvise_v8000_params_st {
849 const void *devPtr;
850 size_t count;
851 enum cudaMemoryAdvise advice;
852 int device;
853} cudaMemAdvise_v8000_params;
854
855typedef struct cudaMemRangeGetAttribute_v8000_params_st {
856 void *data;
857 size_t dataSize;
858 enum cudaMemRangeAttribute attribute;
859 const void *devPtr;
860 size_t count;
861} cudaMemRangeGetAttribute_v8000_params;
862
863typedef struct cudaMemRangeGetAttributes_v8000_params_st {
864 void **data;
865 size_t *dataSizes;
866 enum cudaMemRangeAttribute *attributes;
867 size_t numAttributes;
868 const void *devPtr;
869 size_t count;
870} cudaMemRangeGetAttributes_v8000_params;
871
872typedef struct cudaMemcpyToArray_ptds_v7000_params_st {
873 cudaArray_t dst;
874 size_t wOffset;
875 size_t hOffset;
876 const void *src;
877 size_t count;
878 enum cudaMemcpyKind kind;
879} cudaMemcpyToArray_ptds_v7000_params;
880
881typedef struct cudaMemcpyFromArray_ptds_v7000_params_st {
882 void *dst;
883 cudaArray_const_t src;
884 size_t wOffset;
885 size_t hOffset;
886 size_t count;
887 enum cudaMemcpyKind kind;
888} cudaMemcpyFromArray_ptds_v7000_params;
889
890typedef struct cudaMemcpyArrayToArray_ptds_v7000_params_st {
891 cudaArray_t dst;
892 size_t wOffsetDst;
893 size_t hOffsetDst;
894 cudaArray_const_t src;
895 size_t wOffsetSrc;
896 size_t hOffsetSrc;
897 size_t count;
898 enum cudaMemcpyKind kind;
899} cudaMemcpyArrayToArray_ptds_v7000_params;
900
901typedef struct cudaMemcpyToArrayAsync_ptsz_v7000_params_st {
902 cudaArray_t dst;
903 size_t wOffset;
904 size_t hOffset;
905 const void *src;
906 size_t count;
907 enum cudaMemcpyKind kind;
908 cudaStream_t stream;
909} cudaMemcpyToArrayAsync_ptsz_v7000_params;
910
911typedef struct cudaMemcpyFromArrayAsync_ptsz_v7000_params_st {
912 void *dst;
913 cudaArray_const_t src;
914 size_t wOffset;
915 size_t hOffset;
916 size_t count;
917 enum cudaMemcpyKind kind;
918 cudaStream_t stream;
919} cudaMemcpyFromArrayAsync_ptsz_v7000_params;
920
921typedef struct cudaMallocAsync_ptsz_v11020_params_st {
922 void **devPtr;
923 size_t size;
924 cudaStream_t hStream;
925} cudaMallocAsync_ptsz_v11020_params;
926
927typedef struct cudaFreeAsync_ptsz_v11020_params_st {
928 void *devPtr;
929 cudaStream_t hStream;
930} cudaFreeAsync_ptsz_v11020_params;
931
932typedef struct cudaMemPoolTrimTo_v11020_params_st {
933 cudaMemPool_t memPool;
934 size_t minBytesToKeep;
935} cudaMemPoolTrimTo_v11020_params;
936
937typedef struct cudaMemPoolSetAttribute_v11020_params_st {
938 cudaMemPool_t memPool;
939 enum cudaMemPoolAttr attr;
940 void *value;
941} cudaMemPoolSetAttribute_v11020_params;
942
943typedef struct cudaMemPoolGetAttribute_v11020_params_st {
944 cudaMemPool_t memPool;
945 enum cudaMemPoolAttr attr;
946 void *value;
947} cudaMemPoolGetAttribute_v11020_params;
948
949typedef struct cudaMemPoolSetAccess_v11020_params_st {
950 cudaMemPool_t memPool;
951 const struct cudaMemAccessDesc *descList;
952 size_t count;
953} cudaMemPoolSetAccess_v11020_params;
954
955typedef struct cudaMemPoolGetAccess_v11020_params_st {
956 enum cudaMemAccessFlags *flags;
957 cudaMemPool_t memPool;
958 struct cudaMemLocation *location;
959} cudaMemPoolGetAccess_v11020_params;
960
961typedef struct cudaMemPoolCreate_v11020_params_st {
962 cudaMemPool_t *memPool;
963 const struct cudaMemPoolProps *poolProps;
964} cudaMemPoolCreate_v11020_params;
965
966typedef struct cudaMemPoolDestroy_v11020_params_st {
967 cudaMemPool_t memPool;
968} cudaMemPoolDestroy_v11020_params;
969
970typedef struct cudaMallocFromPoolAsync_ptsz_v11020_params_st {
971 void **ptr;
972 size_t size;
973 cudaMemPool_t memPool;
974 cudaStream_t stream;
975} cudaMallocFromPoolAsync_ptsz_v11020_params;
976
977typedef struct cudaMemPoolExportToShareableHandle_v11020_params_st {
978 void *shareableHandle;
979 cudaMemPool_t memPool;
980 enum cudaMemAllocationHandleType handleType;
981 unsigned int flags;
982} cudaMemPoolExportToShareableHandle_v11020_params;
983
984typedef struct cudaMemPoolImportFromShareableHandle_v11020_params_st {
985 cudaMemPool_t *memPool;
986 void *shareableHandle;
987 enum cudaMemAllocationHandleType handleType;
988 unsigned int flags;
989} cudaMemPoolImportFromShareableHandle_v11020_params;
990
991typedef struct cudaMemPoolExportPointer_v11020_params_st {
992 struct cudaMemPoolPtrExportData *exportData;
993 void *ptr;
994} cudaMemPoolExportPointer_v11020_params;
995
996typedef struct cudaMemPoolImportPointer_v11020_params_st {
997 void **ptr;
998 cudaMemPool_t memPool;
999 struct cudaMemPoolPtrExportData *exportData;
1000} cudaMemPoolImportPointer_v11020_params;
1001
1002typedef struct cudaPointerGetAttributes_v4000_params_st {
1003 struct cudaPointerAttributes *attributes;
1004 const void *ptr;
1005} cudaPointerGetAttributes_v4000_params;
1006
1007typedef struct cudaDeviceCanAccessPeer_v4000_params_st {
1008 int *canAccessPeer;
1009 int device;
1010 int peerDevice;
1011} cudaDeviceCanAccessPeer_v4000_params;
1012
1013typedef struct cudaDeviceEnablePeerAccess_v4000_params_st {
1014 int peerDevice;
1015 unsigned int flags;
1016} cudaDeviceEnablePeerAccess_v4000_params;
1017
1018typedef struct cudaDeviceDisablePeerAccess_v4000_params_st {
1019 int peerDevice;
1020} cudaDeviceDisablePeerAccess_v4000_params;
1021
1022typedef struct cudaGraphicsUnregisterResource_v3020_params_st {
1023 cudaGraphicsResource_t resource;
1024} cudaGraphicsUnregisterResource_v3020_params;
1025
1026typedef struct cudaGraphicsResourceSetMapFlags_v3020_params_st {
1027 cudaGraphicsResource_t resource;
1028 unsigned int flags;
1029} cudaGraphicsResourceSetMapFlags_v3020_params;
1030
1031typedef struct cudaGraphicsMapResources_v3020_params_st {
1032 int count;
1033 cudaGraphicsResource_t *resources;
1034 cudaStream_t stream;
1035} cudaGraphicsMapResources_v3020_params;
1036
1037typedef struct cudaGraphicsUnmapResources_v3020_params_st {
1038 int count;
1039 cudaGraphicsResource_t *resources;
1040 cudaStream_t stream;
1041} cudaGraphicsUnmapResources_v3020_params;
1042
1043typedef struct cudaGraphicsResourceGetMappedPointer_v3020_params_st {
1044 void **devPtr;
1045 size_t *size;
1046 cudaGraphicsResource_t resource;
1047} cudaGraphicsResourceGetMappedPointer_v3020_params;
1048
1049typedef struct cudaGraphicsSubResourceGetMappedArray_v3020_params_st {
1050 cudaArray_t *array;
1051 cudaGraphicsResource_t resource;
1052 unsigned int arrayIndex;
1053 unsigned int mipLevel;
1054} cudaGraphicsSubResourceGetMappedArray_v3020_params;
1055
1056typedef struct cudaGraphicsResourceGetMappedMipmappedArray_v5000_params_st {
1057 cudaMipmappedArray_t *mipmappedArray;
1058 cudaGraphicsResource_t resource;
1059} cudaGraphicsResourceGetMappedMipmappedArray_v5000_params;
1060
1061typedef struct cudaBindTexture_v3020_params_st {
1062 size_t *offset;
1063 const struct textureReference *texref;
1064 const void *devPtr;
1065 const struct cudaChannelFormatDesc *desc;
1066 size_t size;
1067} cudaBindTexture_v3020_params;
1068
1069typedef struct cudaBindTexture2D_v3020_params_st {
1070 size_t *offset;
1071 const struct textureReference *texref;
1072 const void *devPtr;
1073 const struct cudaChannelFormatDesc *desc;
1074 size_t width;
1075 size_t height;
1076 size_t pitch;
1077} cudaBindTexture2D_v3020_params;
1078
1079typedef struct cudaBindTextureToArray_v3020_params_st {
1080 const struct textureReference *texref;
1081 cudaArray_const_t array;
1082 const struct cudaChannelFormatDesc *desc;
1083} cudaBindTextureToArray_v3020_params;
1084
1085typedef struct cudaBindTextureToMipmappedArray_v5000_params_st {
1086 const struct textureReference *texref;
1087 cudaMipmappedArray_const_t mipmappedArray;
1088 const struct cudaChannelFormatDesc *desc;
1089} cudaBindTextureToMipmappedArray_v5000_params;
1090
1091typedef struct cudaUnbindTexture_v3020_params_st {
1092 const struct textureReference *texref;
1093} cudaUnbindTexture_v3020_params;
1094
1095typedef struct cudaGetTextureAlignmentOffset_v3020_params_st {
1096 size_t *offset;
1097 const struct textureReference *texref;
1098} cudaGetTextureAlignmentOffset_v3020_params;
1099
1100typedef struct cudaGetTextureReference_v3020_params_st {
1101 const struct textureReference **texref;
1102 const void *symbol;
1103} cudaGetTextureReference_v3020_params;
1104
1105typedef struct cudaBindSurfaceToArray_v3020_params_st {
1106 const struct surfaceReference *surfref;
1107 cudaArray_const_t array;
1108 const struct cudaChannelFormatDesc *desc;
1109} cudaBindSurfaceToArray_v3020_params;
1110
1111typedef struct cudaGetSurfaceReference_v3020_params_st {
1112 const struct surfaceReference **surfref;
1113 const void *symbol;
1114} cudaGetSurfaceReference_v3020_params;
1115
1116typedef struct cudaGetChannelDesc_v3020_params_st {
1117 struct cudaChannelFormatDesc *desc;
1118 cudaArray_const_t array;
1119} cudaGetChannelDesc_v3020_params;
1120
1121typedef struct cudaCreateChannelDesc_v3020_params_st {
1122 int x;
1123 int y;
1124 int z;
1125 int w;
1126 enum cudaChannelFormatKind f;
1127} cudaCreateChannelDesc_v3020_params;
1128
1129typedef struct cudaCreateTextureObject_v5000_params_st {
1130 cudaTextureObject_t *pTexObject;
1131 const struct cudaResourceDesc *pResDesc;
1132 const struct cudaTextureDesc *pTexDesc;
1133 const struct cudaResourceViewDesc *pResViewDesc;
1134} cudaCreateTextureObject_v5000_params;
1135
1136typedef struct cudaDestroyTextureObject_v5000_params_st {
1137 cudaTextureObject_t texObject;
1138} cudaDestroyTextureObject_v5000_params;
1139
1140typedef struct cudaGetTextureObjectResourceDesc_v5000_params_st {
1141 struct cudaResourceDesc *pResDesc;
1142 cudaTextureObject_t texObject;
1143} cudaGetTextureObjectResourceDesc_v5000_params;
1144
1145typedef struct cudaGetTextureObjectTextureDesc_v5000_params_st {
1146 struct cudaTextureDesc *pTexDesc;
1147 cudaTextureObject_t texObject;
1148} cudaGetTextureObjectTextureDesc_v5000_params;
1149
1150typedef struct cudaGetTextureObjectResourceViewDesc_v5000_params_st {
1151 struct cudaResourceViewDesc *pResViewDesc;
1152 cudaTextureObject_t texObject;
1153} cudaGetTextureObjectResourceViewDesc_v5000_params;
1154
1155typedef struct cudaCreateSurfaceObject_v5000_params_st {
1156 cudaSurfaceObject_t *pSurfObject;
1157 const struct cudaResourceDesc *pResDesc;
1158} cudaCreateSurfaceObject_v5000_params;
1159
1160typedef struct cudaDestroySurfaceObject_v5000_params_st {
1161 cudaSurfaceObject_t surfObject;
1162} cudaDestroySurfaceObject_v5000_params;
1163
1164typedef struct cudaGetSurfaceObjectResourceDesc_v5000_params_st {
1165 struct cudaResourceDesc *pResDesc;
1166 cudaSurfaceObject_t surfObject;
1167} cudaGetSurfaceObjectResourceDesc_v5000_params;
1168
1169typedef struct cudaDriverGetVersion_v3020_params_st {
1170 int *driverVersion;
1171} cudaDriverGetVersion_v3020_params;
1172
1173typedef struct cudaRuntimeGetVersion_v3020_params_st {
1174 int *runtimeVersion;
1175} cudaRuntimeGetVersion_v3020_params;
1176
1177typedef struct cudaGraphCreate_v10000_params_st {
1178 cudaGraph_t *pGraph;
1179 unsigned int flags;
1180} cudaGraphCreate_v10000_params;
1181
1182typedef struct cudaGraphAddKernelNode_v10000_params_st {
1183 cudaGraphNode_t *pGraphNode;
1184 cudaGraph_t graph;
1185 const cudaGraphNode_t *pDependencies;
1186 size_t numDependencies;
1187 const struct cudaKernelNodeParams *pNodeParams;
1188} cudaGraphAddKernelNode_v10000_params;
1189
1190typedef struct cudaGraphKernelNodeGetParams_v10000_params_st {
1191 cudaGraphNode_t node;
1192 struct cudaKernelNodeParams *pNodeParams;
1193} cudaGraphKernelNodeGetParams_v10000_params;
1194
1195typedef struct cudaGraphKernelNodeSetParams_v10000_params_st {
1196 cudaGraphNode_t node;
1197 const struct cudaKernelNodeParams *pNodeParams;
1198} cudaGraphKernelNodeSetParams_v10000_params;
1199
1200typedef struct cudaGraphKernelNodeCopyAttributes_v11000_params_st {