Coverage for cuda/bindings/_internal/driver.pyx: 66.97%

1# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. (empty)

2# 

3# SPDX-License-Identifier: Apache-2.0 

4# 

5# This code was automatically generated across versions from 12.9.0 to 13.4.1. Do not modify it directly. 

6# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=c6a477ceb1a35675c0ffe5e40f9826ea3e3bd9cbec23720f78fe4cf28feafbe0 

7  

8  

9# <<<< PREAMBLE CONTENT >>>> 

10  

11cdef extern from * nogil: 

12 """ 

13 #if defined(_MSC_VER) && !defined(__clang__) 

14 #include <intrin.h> 

15 static __forceinline int atomic_int_load(int *p) { 

16 int v = *(int volatile *)p; _ReadBarrier(); return v; 

17 } 

18 static __forceinline void atomic_int_store(int *p, int v) { 

19 _WriteBarrier(); *(int volatile *)p = v; 

20 } 

21 #elif defined(__cplusplus) 

22 /* GCC/Clang __atomic builtins work in any C++ standard without headers */ 

23 static inline int atomic_int_load(int *p) { 

24 return __atomic_load_n(p, __ATOMIC_ACQUIRE); 

25 } 

26 static inline void atomic_int_store(int *p, int v) { 

27 __atomic_store_n(p, v, __ATOMIC_RELEASE); 

28 } 

29 #else 

30 #include <stdatomic.h> 

31 static inline int atomic_int_load(int *p) { 

32 return (int)atomic_load_explicit((atomic_int *)p, memory_order_acquire); 

33 } 

34 static inline void atomic_int_store(int *p, int v) { 

35 atomic_store_explicit((atomic_int *)p, v, memory_order_release); 

36 } 

37 #endif 

38  

39 """ 

40 cdef int _cyb_atomic_int_load "atomic_int_load"(int *p) nogil 

41 cdef void _cyb_atomic_int_store "atomic_int_store"(int *p, int v) nogil 

42  

43cdef extern from "<dlfcn.h>": 

44 void* _cyb_dlsym "dlsym"(void*, const char*) nogil 

45  

46from libc.stdint cimport intptr_t 

47  

48from os import getenv as _cyb_getenv (empty)

49import threading as _cyb_threading (empty)

50  

51ctypedef int (*_cyb_cuGetProcAddress_v2_T)(const char *, void **, int, cuuint64_t, CUdriverProcAddressQueryResult *)except?CUDA_ERROR_NOT_FOUND nogil 

52  

53cdef int _cyb___py_driver_init = 0 (empty)

54cdef dict _cyb_func_ptrs = None (empty)

55cdef object _cyb_symbol_lock = _cyb_threading.Lock() (empty)

56  

57# <<<< END OF PREAMBLE CONTENT >>>> 

58  

59from libc.stdint cimport uintptr_t 

60  

61from .utils import FunctionNotFoundError, NotSupportedError (empty)

62from cuda.pathfinder import load_nvidia_dynamic_lib (empty)

63  

64  

65############################################################################### 

66# Wrapper init 

67############################################################################### 

68  

69  

70cdef void* __cuGetErrorString = NULL (empty)

71cdef void* __cuGetErrorName = NULL (empty)

72cdef void* __cuInit = NULL (empty)

73cdef void* __cuDriverGetVersion = NULL (empty)

74cdef void* __cuDeviceGet = NULL (empty)

75cdef void* __cuDeviceGetCount = NULL (empty)

76cdef void* __cuDeviceGetName = NULL (empty)

77cdef void* __cuDeviceGetUuid_v2 = NULL (empty)

78cdef void* __cuDeviceGetLuid = NULL (empty)

79cdef void* __cuDeviceTotalMem_v2 = NULL (empty)

80cdef void* __cuDeviceGetTexture1DLinearMaxWidth = NULL (empty)

81cdef void* __cuDeviceGetAttribute = NULL (empty)

82cdef void* __cuDeviceGetNvSciSyncAttributes = NULL (empty)

83cdef void* __cuDeviceSetMemPool = NULL (empty)

84cdef void* __cuDeviceGetMemPool = NULL (empty)

85cdef void* __cuDeviceGetDefaultMemPool = NULL (empty)

86cdef void* __cuDeviceGetExecAffinitySupport = NULL (empty)

87cdef void* __cuFlushGPUDirectRDMAWrites = NULL (empty)

88cdef void* __cuDeviceGetProperties = NULL (empty)

89cdef void* __cuDeviceComputeCapability = NULL (empty)

90cdef void* __cuDevicePrimaryCtxRetain = NULL (empty)

91cdef void* __cuDevicePrimaryCtxRelease_v2 = NULL (empty)

92cdef void* __cuDevicePrimaryCtxSetFlags_v2 = NULL (empty)

93cdef void* __cuDevicePrimaryCtxGetState = NULL (empty)

94cdef void* __cuDevicePrimaryCtxReset_v2 = NULL (empty)

95cdef void* __cuCtxCreate_v2 = NULL (empty)

96cdef void* __cuCtxCreate_v3 = NULL (empty)

97cdef void* __cuCtxCreate_v4 = NULL (empty)

98cdef void* __cuCtxDestroy_v2 = NULL (empty)

99cdef void* __cuCtxPushCurrent_v2 = NULL (empty)

100cdef void* __cuCtxPopCurrent_v2 = NULL (empty)

101cdef void* __cuCtxSetCurrent = NULL (empty)

102cdef void* __cuCtxGetCurrent = NULL (empty)

103cdef void* __cuCtxGetDevice = NULL (empty)

104cdef void* __cuCtxGetFlags = NULL (empty)

105cdef void* __cuCtxSetFlags = NULL (empty)

106cdef void* __cuCtxGetId = NULL (empty)

107cdef void* __cuCtxSynchronize = NULL (empty)

108cdef void* __cuCtxSetLimit = NULL (empty)

109cdef void* __cuCtxGetLimit = NULL (empty)

110cdef void* __cuCtxGetCacheConfig = NULL (empty)

111cdef void* __cuCtxSetCacheConfig = NULL (empty)

112cdef void* __cuCtxGetApiVersion = NULL (empty)

113cdef void* __cuCtxGetStreamPriorityRange = NULL (empty)

114cdef void* __cuCtxResetPersistingL2Cache = NULL (empty)

115cdef void* __cuCtxGetExecAffinity = NULL (empty)

116cdef void* __cuCtxRecordEvent = NULL (empty)

117cdef void* __cuCtxWaitEvent = NULL (empty)

118cdef void* __cuCtxAttach = NULL (empty)

119cdef void* __cuCtxDetach = NULL (empty)

120cdef void* __cuCtxGetSharedMemConfig = NULL (empty)

121cdef void* __cuCtxSetSharedMemConfig = NULL (empty)

122cdef void* __cuModuleLoad = NULL (empty)

123cdef void* __cuModuleLoadData = NULL (empty)

124cdef void* __cuModuleLoadDataEx = NULL (empty)

125cdef void* __cuModuleLoadFatBinary = NULL (empty)

126cdef void* __cuModuleUnload = NULL (empty)

127cdef void* __cuModuleGetLoadingMode = NULL (empty)

128cdef void* __cuModuleGetFunction = NULL (empty)

129cdef void* __cuModuleGetFunctionCount = NULL (empty)

130cdef void* __cuModuleEnumerateFunctions = NULL (empty)

131cdef void* __cuModuleGetGlobal_v2 = NULL (empty)

132cdef void* __cuLinkCreate_v2 = NULL (empty)

133cdef void* __cuLinkAddData_v2 = NULL (empty)

134cdef void* __cuLinkAddFile_v2 = NULL (empty)

135cdef void* __cuLinkComplete = NULL (empty)

136cdef void* __cuLinkDestroy = NULL (empty)

137cdef void* __cuModuleGetTexRef = NULL (empty)

138cdef void* __cuModuleGetSurfRef = NULL (empty)

139cdef void* __cuLibraryLoadData = NULL (empty)

140cdef void* __cuLibraryLoadFromFile = NULL (empty)

141cdef void* __cuLibraryUnload = NULL (empty)

142cdef void* __cuLibraryGetKernel = NULL (empty)

143cdef void* __cuLibraryGetKernelCount = NULL (empty)

144cdef void* __cuLibraryEnumerateKernels = NULL (empty)

145cdef void* __cuLibraryGetModule = NULL (empty)

146cdef void* __cuKernelGetFunction = NULL (empty)

147cdef void* __cuKernelGetLibrary = NULL (empty)

148cdef void* __cuLibraryGetGlobal = NULL (empty)

149cdef void* __cuLibraryGetManaged = NULL (empty)

150cdef void* __cuLibraryGetUnifiedFunction = NULL (empty)

151cdef void* __cuKernelGetAttribute = NULL (empty)

152cdef void* __cuKernelSetAttribute = NULL (empty)

153cdef void* __cuKernelSetCacheConfig = NULL (empty)

154cdef void* __cuKernelGetName = NULL (empty)

155cdef void* __cuKernelGetParamInfo = NULL (empty)

156cdef void* __cuMemGetInfo_v2 = NULL (empty)

157cdef void* __cuMemAlloc_v2 = NULL (empty)

158cdef void* __cuMemAllocPitch_v2 = NULL (empty)

159cdef void* __cuMemFree_v2 = NULL (empty)

160cdef void* __cuMemGetAddressRange_v2 = NULL (empty)

161cdef void* __cuMemAllocHost_v2 = NULL (empty)

162cdef void* __cuMemFreeHost = NULL (empty)

163cdef void* __cuMemHostAlloc = NULL (empty)

164cdef void* __cuMemHostGetDevicePointer_v2 = NULL (empty)

165cdef void* __cuMemHostGetFlags = NULL (empty)

166cdef void* __cuMemAllocManaged = NULL (empty)

167cdef void* __cuDeviceRegisterAsyncNotification = NULL (empty)

168cdef void* __cuDeviceUnregisterAsyncNotification = NULL (empty)

169cdef void* __cuDeviceGetByPCIBusId = NULL (empty)

170cdef void* __cuDeviceGetPCIBusId = NULL (empty)

171cdef void* __cuIpcGetEventHandle = NULL (empty)

172cdef void* __cuIpcOpenEventHandle = NULL (empty)

173cdef void* __cuIpcGetMemHandle = NULL (empty)

174cdef void* __cuIpcOpenMemHandle_v2 = NULL (empty)

175cdef void* __cuIpcCloseMemHandle = NULL (empty)

176cdef void* __cuMemHostRegister_v2 = NULL (empty)

177cdef void* __cuMemHostUnregister = NULL (empty)

178cdef void* __cuMemcpy = NULL (empty)

179cdef void* __cuMemcpyPeer = NULL (empty)

180cdef void* __cuMemcpyHtoD_v2 = NULL (empty)

181cdef void* __cuMemcpyDtoH_v2 = NULL (empty)

182cdef void* __cuMemcpyDtoD_v2 = NULL (empty)

183cdef void* __cuMemcpyDtoA_v2 = NULL (empty)

184cdef void* __cuMemcpyAtoD_v2 = NULL (empty)

185cdef void* __cuMemcpyHtoA_v2 = NULL (empty)

186cdef void* __cuMemcpyAtoH_v2 = NULL (empty)

187cdef void* __cuMemcpyAtoA_v2 = NULL (empty)

188cdef void* __cuMemcpy2D_v2 = NULL (empty)

189cdef void* __cuMemcpy2DUnaligned_v2 = NULL (empty)

190cdef void* __cuMemcpy3D_v2 = NULL (empty)

191cdef void* __cuMemcpy3DPeer = NULL (empty)

192cdef void* __cuMemcpyAsync = NULL (empty)

193cdef void* __cuMemcpyPeerAsync = NULL (empty)

194cdef void* __cuMemcpyHtoDAsync_v2 = NULL (empty)

195cdef void* __cuMemcpyDtoHAsync_v2 = NULL (empty)

196cdef void* __cuMemcpyDtoDAsync_v2 = NULL (empty)

197cdef void* __cuMemcpyHtoAAsync_v2 = NULL (empty)

198cdef void* __cuMemcpyAtoHAsync_v2 = NULL (empty)

199cdef void* __cuMemcpy2DAsync_v2 = NULL (empty)

200cdef void* __cuMemcpy3DAsync_v2 = NULL (empty)

201cdef void* __cuMemcpy3DPeerAsync = NULL (empty)

202cdef void* __cuMemsetD8_v2 = NULL (empty)

203cdef void* __cuMemsetD16_v2 = NULL (empty)

204cdef void* __cuMemsetD32_v2 = NULL (empty)

205cdef void* __cuMemsetD2D8_v2 = NULL (empty)

206cdef void* __cuMemsetD2D16_v2 = NULL (empty)

207cdef void* __cuMemsetD2D32_v2 = NULL (empty)

208cdef void* __cuMemsetD8Async = NULL (empty)

209cdef void* __cuMemsetD16Async = NULL (empty)

210cdef void* __cuMemsetD32Async = NULL (empty)

211cdef void* __cuMemsetD2D8Async = NULL (empty)

212cdef void* __cuMemsetD2D16Async = NULL (empty)

213cdef void* __cuMemsetD2D32Async = NULL (empty)

214cdef void* __cuArrayCreate_v2 = NULL (empty)

215cdef void* __cuArrayGetDescriptor_v2 = NULL (empty)

216cdef void* __cuArrayGetSparseProperties = NULL (empty)

217cdef void* __cuMipmappedArrayGetSparseProperties = NULL (empty)

218cdef void* __cuArrayGetMemoryRequirements = NULL (empty)

219cdef void* __cuMipmappedArrayGetMemoryRequirements = NULL (empty)

220cdef void* __cuArrayGetPlane = NULL (empty)

221cdef void* __cuArrayDestroy = NULL (empty)

222cdef void* __cuArray3DCreate_v2 = NULL (empty)

223cdef void* __cuArray3DGetDescriptor_v2 = NULL (empty)

224cdef void* __cuMipmappedArrayCreate = NULL (empty)

225cdef void* __cuMipmappedArrayGetLevel = NULL (empty)

226cdef void* __cuMipmappedArrayDestroy = NULL (empty)

227cdef void* __cuMemGetHandleForAddressRange = NULL (empty)

228cdef void* __cuMemBatchDecompressAsync = NULL (empty)

229cdef void* __cuMemAddressReserve = NULL (empty)

230cdef void* __cuMemAddressFree = NULL (empty)

231cdef void* __cuMemCreate = NULL (empty)

232cdef void* __cuMemRelease = NULL (empty)

233cdef void* __cuMemMap = NULL (empty)

234cdef void* __cuMemMapArrayAsync = NULL (empty)

235cdef void* __cuMemUnmap = NULL (empty)

236cdef void* __cuMemSetAccess = NULL (empty)

237cdef void* __cuMemGetAccess = NULL (empty)

238cdef void* __cuMemExportToShareableHandle = NULL (empty)

239cdef void* __cuMemImportFromShareableHandle = NULL (empty)

240cdef void* __cuMemGetAllocationGranularity = NULL (empty)

241cdef void* __cuMemGetAllocationPropertiesFromHandle = NULL (empty)

242cdef void* __cuMemRetainAllocationHandle = NULL (empty)

243cdef void* __cuMemFreeAsync = NULL (empty)

244cdef void* __cuMemAllocAsync = NULL (empty)

245cdef void* __cuMemPoolTrimTo = NULL (empty)

246cdef void* __cuMemPoolSetAttribute = NULL (empty)

247cdef void* __cuMemPoolGetAttribute = NULL (empty)

248cdef void* __cuMemPoolSetAccess = NULL (empty)

249cdef void* __cuMemPoolGetAccess = NULL (empty)

250cdef void* __cuMemPoolCreate = NULL (empty)

251cdef void* __cuMemPoolDestroy = NULL (empty)

252cdef void* __cuMemAllocFromPoolAsync = NULL (empty)

253cdef void* __cuMemPoolExportToShareableHandle = NULL (empty)

254cdef void* __cuMemPoolImportFromShareableHandle = NULL (empty)

255cdef void* __cuMemPoolExportPointer = NULL (empty)

256cdef void* __cuMemPoolImportPointer = NULL (empty)

257cdef void* __cuMulticastCreate = NULL (empty)

258cdef void* __cuMulticastAddDevice = NULL (empty)

259cdef void* __cuMulticastBindMem = NULL (empty)

260cdef void* __cuMulticastBindAddr = NULL (empty)

261cdef void* __cuMulticastUnbind = NULL (empty)

262cdef void* __cuMulticastGetGranularity = NULL (empty)

263cdef void* __cuPointerGetAttribute = NULL (empty)

264cdef void* __cuMemPrefetchAsync_v2 = NULL (empty)

265cdef void* __cuMemAdvise_v2 = NULL (empty)

266cdef void* __cuMemRangeGetAttribute = NULL (empty)

267cdef void* __cuMemRangeGetAttributes = NULL (empty)

268cdef void* __cuPointerSetAttribute = NULL (empty)

269cdef void* __cuPointerGetAttributes = NULL (empty)

270cdef void* __cuStreamCreate = NULL (empty)

271cdef void* __cuStreamCreateWithPriority = NULL (empty)

272cdef void* __cuStreamGetPriority = NULL (empty)

273cdef void* __cuStreamGetDevice = NULL (empty)

274cdef void* __cuStreamGetFlags = NULL (empty)

275cdef void* __cuStreamGetId = NULL (empty)

276cdef void* __cuStreamGetCtx = NULL (empty)

277cdef void* __cuStreamGetCtx_v2 = NULL (empty)

278cdef void* __cuStreamWaitEvent = NULL (empty)

279cdef void* __cuStreamAddCallback = NULL (empty)

280cdef void* __cuStreamBeginCapture_v2 = NULL (empty)

281cdef void* __cuStreamBeginCaptureToGraph = NULL (empty)

282cdef void* __cuThreadExchangeStreamCaptureMode = NULL (empty)

283cdef void* __cuStreamEndCapture = NULL (empty)

284cdef void* __cuStreamIsCapturing = NULL (empty)

285cdef void* __cuStreamGetCaptureInfo_v2 = NULL (empty)

286cdef void* __cuStreamGetCaptureInfo_v3 = NULL (empty)

287cdef void* __cuStreamUpdateCaptureDependencies_v2 = NULL (empty)

288cdef void* __cuStreamAttachMemAsync = NULL (empty)

289cdef void* __cuStreamQuery = NULL (empty)

290cdef void* __cuStreamSynchronize = NULL (empty)

291cdef void* __cuStreamDestroy_v2 = NULL (empty)

292cdef void* __cuStreamCopyAttributes = NULL (empty)

293cdef void* __cuStreamGetAttribute = NULL (empty)

294cdef void* __cuStreamSetAttribute = NULL (empty)

295cdef void* __cuEventCreate = NULL (empty)

296cdef void* __cuEventRecord = NULL (empty)

297cdef void* __cuEventRecordWithFlags = NULL (empty)

298cdef void* __cuEventQuery = NULL (empty)

299cdef void* __cuEventSynchronize = NULL (empty)

300cdef void* __cuEventDestroy_v2 = NULL (empty)

301cdef void* __cuEventElapsedTime_v2 = NULL (empty)

302cdef void* __cuImportExternalMemory = NULL (empty)

303cdef void* __cuExternalMemoryGetMappedBuffer = NULL (empty)

304cdef void* __cuExternalMemoryGetMappedMipmappedArray = NULL (empty)

305cdef void* __cuDestroyExternalMemory = NULL (empty)

306cdef void* __cuImportExternalSemaphore = NULL (empty)

307cdef void* __cuSignalExternalSemaphoresAsync = NULL (empty)

308cdef void* __cuWaitExternalSemaphoresAsync = NULL (empty)

309cdef void* __cuDestroyExternalSemaphore = NULL (empty)

310cdef void* __cuStreamWaitValue32_v2 = NULL (empty)

311cdef void* __cuStreamWaitValue64_v2 = NULL (empty)

312cdef void* __cuStreamWriteValue32_v2 = NULL (empty)

313cdef void* __cuStreamWriteValue64_v2 = NULL (empty)

314cdef void* __cuStreamBatchMemOp_v2 = NULL (empty)

315cdef void* __cuFuncGetAttribute = NULL (empty)

316cdef void* __cuFuncSetAttribute = NULL (empty)

317cdef void* __cuFuncSetCacheConfig = NULL (empty)

318cdef void* __cuFuncGetModule = NULL (empty)

319cdef void* __cuFuncGetName = NULL (empty)

320cdef void* __cuFuncGetParamInfo = NULL (empty)

321cdef void* __cuFuncIsLoaded = NULL (empty)

322cdef void* __cuFuncLoad = NULL (empty)

323cdef void* __cuLaunchKernel = NULL (empty)

324cdef void* __cuLaunchKernelEx = NULL (empty)

325cdef void* __cuLaunchCooperativeKernel = NULL (empty)

326cdef void* __cuLaunchCooperativeKernelMultiDevice = NULL (empty)

327cdef void* __cuLaunchHostFunc = NULL (empty)

328cdef void* __cuFuncSetBlockShape = NULL (empty)

329cdef void* __cuFuncSetSharedSize = NULL (empty)

330cdef void* __cuParamSetSize = NULL (empty)

331cdef void* __cuParamSeti = NULL (empty)

332cdef void* __cuParamSetf = NULL (empty)

333cdef void* __cuParamSetv = NULL (empty)

334cdef void* __cuLaunch = NULL (empty)

335cdef void* __cuLaunchGrid = NULL (empty)

336cdef void* __cuLaunchGridAsync = NULL (empty)

337cdef void* __cuParamSetTexRef = NULL (empty)

338cdef void* __cuFuncSetSharedMemConfig = NULL (empty)

339cdef void* __cuGraphCreate = NULL (empty)

340cdef void* __cuGraphAddKernelNode_v2 = NULL (empty)

341cdef void* __cuGraphKernelNodeGetParams_v2 = NULL (empty)

342cdef void* __cuGraphKernelNodeSetParams_v2 = NULL (empty)

343cdef void* __cuGraphAddMemcpyNode = NULL (empty)

344cdef void* __cuGraphMemcpyNodeGetParams = NULL (empty)

345cdef void* __cuGraphMemcpyNodeSetParams = NULL (empty)

346cdef void* __cuGraphAddMemsetNode = NULL (empty)

347cdef void* __cuGraphMemsetNodeGetParams = NULL (empty)

348cdef void* __cuGraphMemsetNodeSetParams = NULL (empty)

349cdef void* __cuGraphAddHostNode = NULL (empty)

350cdef void* __cuGraphHostNodeGetParams = NULL (empty)

351cdef void* __cuGraphHostNodeSetParams = NULL (empty)

352cdef void* __cuGraphAddChildGraphNode = NULL (empty)

353cdef void* __cuGraphChildGraphNodeGetGraph = NULL (empty)

354cdef void* __cuGraphAddEmptyNode = NULL (empty)

355cdef void* __cuGraphAddEventRecordNode = NULL (empty)

356cdef void* __cuGraphEventRecordNodeGetEvent = NULL (empty)

357cdef void* __cuGraphEventRecordNodeSetEvent = NULL (empty)

358cdef void* __cuGraphAddEventWaitNode = NULL (empty)

359cdef void* __cuGraphEventWaitNodeGetEvent = NULL (empty)

360cdef void* __cuGraphEventWaitNodeSetEvent = NULL (empty)

361cdef void* __cuGraphAddExternalSemaphoresSignalNode = NULL (empty)

362cdef void* __cuGraphExternalSemaphoresSignalNodeGetParams = NULL (empty)

363cdef void* __cuGraphExternalSemaphoresSignalNodeSetParams = NULL (empty)

364cdef void* __cuGraphAddExternalSemaphoresWaitNode = NULL (empty)

365cdef void* __cuGraphExternalSemaphoresWaitNodeGetParams = NULL (empty)

366cdef void* __cuGraphExternalSemaphoresWaitNodeSetParams = NULL (empty)

367cdef void* __cuGraphAddBatchMemOpNode = NULL (empty)

368cdef void* __cuGraphBatchMemOpNodeGetParams = NULL (empty)

369cdef void* __cuGraphBatchMemOpNodeSetParams = NULL (empty)

370cdef void* __cuGraphExecBatchMemOpNodeSetParams = NULL (empty)

371cdef void* __cuGraphAddMemAllocNode = NULL (empty)

372cdef void* __cuGraphMemAllocNodeGetParams = NULL (empty)

373cdef void* __cuGraphAddMemFreeNode = NULL (empty)

374cdef void* __cuGraphMemFreeNodeGetParams = NULL (empty)

375cdef void* __cuDeviceGraphMemTrim = NULL (empty)

376cdef void* __cuDeviceGetGraphMemAttribute = NULL (empty)

377cdef void* __cuDeviceSetGraphMemAttribute = NULL (empty)

378cdef void* __cuGraphClone = NULL (empty)

379cdef void* __cuGraphNodeFindInClone = NULL (empty)

380cdef void* __cuGraphNodeGetType = NULL (empty)

381cdef void* __cuGraphGetNodes = NULL (empty)

382cdef void* __cuGraphGetRootNodes = NULL (empty)

383cdef void* __cuGraphGetEdges_v2 = NULL (empty)

384cdef void* __cuGraphNodeGetDependencies_v2 = NULL (empty)

385cdef void* __cuGraphNodeGetDependentNodes_v2 = NULL (empty)

386cdef void* __cuGraphAddDependencies_v2 = NULL (empty)

387cdef void* __cuGraphRemoveDependencies_v2 = NULL (empty)

388cdef void* __cuGraphDestroyNode = NULL (empty)

389cdef void* __cuGraphInstantiateWithFlags = NULL (empty)

390cdef void* __cuGraphInstantiateWithParams = NULL (empty)

391cdef void* __cuGraphExecGetFlags = NULL (empty)

392cdef void* __cuGraphExecKernelNodeSetParams_v2 = NULL (empty)

393cdef void* __cuGraphExecMemcpyNodeSetParams = NULL (empty)

394cdef void* __cuGraphExecMemsetNodeSetParams = NULL (empty)

395cdef void* __cuGraphExecHostNodeSetParams = NULL (empty)

396cdef void* __cuGraphExecChildGraphNodeSetParams = NULL (empty)

397cdef void* __cuGraphExecEventRecordNodeSetEvent = NULL (empty)

398cdef void* __cuGraphExecEventWaitNodeSetEvent = NULL (empty)

399cdef void* __cuGraphExecExternalSemaphoresSignalNodeSetParams = NULL (empty)

400cdef void* __cuGraphExecExternalSemaphoresWaitNodeSetParams = NULL (empty)

401cdef void* __cuGraphNodeSetEnabled = NULL (empty)

402cdef void* __cuGraphNodeGetEnabled = NULL (empty)

403cdef void* __cuGraphUpload = NULL (empty)

404cdef void* __cuGraphLaunch = NULL (empty)

405cdef void* __cuGraphExecDestroy = NULL (empty)

406cdef void* __cuGraphDestroy = NULL (empty)

407cdef void* __cuGraphExecUpdate_v2 = NULL (empty)

408cdef void* __cuGraphKernelNodeCopyAttributes = NULL (empty)

409cdef void* __cuGraphKernelNodeGetAttribute = NULL (empty)

410cdef void* __cuGraphKernelNodeSetAttribute = NULL (empty)

411cdef void* __cuGraphDebugDotPrint = NULL (empty)

412cdef void* __cuUserObjectCreate = NULL (empty)

413cdef void* __cuUserObjectRetain = NULL (empty)

414cdef void* __cuUserObjectRelease = NULL (empty)

415cdef void* __cuGraphRetainUserObject = NULL (empty)

416cdef void* __cuGraphReleaseUserObject = NULL (empty)

417cdef void* __cuGraphAddNode_v2 = NULL (empty)

418cdef void* __cuGraphNodeSetParams = NULL (empty)

419cdef void* __cuGraphExecNodeSetParams = NULL (empty)

420cdef void* __cuGraphConditionalHandleCreate = NULL (empty)

421cdef void* __cuOccupancyMaxActiveBlocksPerMultiprocessor = NULL (empty)

422cdef void* __cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags = NULL (empty)

423cdef void* __cuOccupancyMaxPotentialBlockSize = NULL (empty)

424cdef void* __cuOccupancyMaxPotentialBlockSizeWithFlags = NULL (empty)

425cdef void* __cuOccupancyAvailableDynamicSMemPerBlock = NULL (empty)

426cdef void* __cuOccupancyMaxPotentialClusterSize = NULL (empty)

427cdef void* __cuOccupancyMaxActiveClusters = NULL (empty)

428cdef void* __cuTexRefSetArray = NULL (empty)

429cdef void* __cuTexRefSetMipmappedArray = NULL (empty)

430cdef void* __cuTexRefSetAddress_v2 = NULL (empty)

431cdef void* __cuTexRefSetAddress2D_v3 = NULL (empty)

432cdef void* __cuTexRefSetFormat = NULL (empty)

433cdef void* __cuTexRefSetAddressMode = NULL (empty)

434cdef void* __cuTexRefSetFilterMode = NULL (empty)

435cdef void* __cuTexRefSetMipmapFilterMode = NULL (empty)

436cdef void* __cuTexRefSetMipmapLevelBias = NULL (empty)

437cdef void* __cuTexRefSetMipmapLevelClamp = NULL (empty)

438cdef void* __cuTexRefSetMaxAnisotropy = NULL (empty)

439cdef void* __cuTexRefSetBorderColor = NULL (empty)

440cdef void* __cuTexRefSetFlags = NULL (empty)

441cdef void* __cuTexRefGetAddress_v2 = NULL (empty)

442cdef void* __cuTexRefGetArray = NULL (empty)

443cdef void* __cuTexRefGetMipmappedArray = NULL (empty)

444cdef void* __cuTexRefGetAddressMode = NULL (empty)

445cdef void* __cuTexRefGetFilterMode = NULL (empty)

446cdef void* __cuTexRefGetFormat = NULL (empty)

447cdef void* __cuTexRefGetMipmapFilterMode = NULL (empty)

448cdef void* __cuTexRefGetMipmapLevelBias = NULL (empty)

449cdef void* __cuTexRefGetMipmapLevelClamp = NULL (empty)

450cdef void* __cuTexRefGetMaxAnisotropy = NULL (empty)

451cdef void* __cuTexRefGetBorderColor = NULL (empty)

452cdef void* __cuTexRefGetFlags = NULL (empty)

453cdef void* __cuTexRefCreate = NULL (empty)

454cdef void* __cuTexRefDestroy = NULL (empty)

455cdef void* __cuSurfRefSetArray = NULL (empty)

456cdef void* __cuSurfRefGetArray = NULL (empty)

457cdef void* __cuTexObjectCreate = NULL (empty)

458cdef void* __cuTexObjectDestroy = NULL (empty)

459cdef void* __cuTexObjectGetResourceDesc = NULL (empty)

460cdef void* __cuTexObjectGetTextureDesc = NULL (empty)

461cdef void* __cuTexObjectGetResourceViewDesc = NULL (empty)

462cdef void* __cuSurfObjectCreate = NULL (empty)

463cdef void* __cuSurfObjectDestroy = NULL (empty)

464cdef void* __cuSurfObjectGetResourceDesc = NULL (empty)

465cdef void* __cuTensorMapEncodeTiled = NULL (empty)

466cdef void* __cuTensorMapEncodeIm2col = NULL (empty)

467cdef void* __cuTensorMapEncodeIm2colWide = NULL (empty)

468cdef void* __cuTensorMapReplaceAddress = NULL (empty)

469cdef void* __cuDeviceCanAccessPeer = NULL (empty)

470cdef void* __cuCtxEnablePeerAccess = NULL (empty)

471cdef void* __cuCtxDisablePeerAccess = NULL (empty)

472cdef void* __cuDeviceGetP2PAttribute = NULL (empty)

473cdef void* __cuGraphicsUnregisterResource = NULL (empty)

474cdef void* __cuGraphicsSubResourceGetMappedArray = NULL (empty)

475cdef void* __cuGraphicsResourceGetMappedMipmappedArray = NULL (empty)

476cdef void* __cuGraphicsResourceGetMappedPointer_v2 = NULL (empty)

477cdef void* __cuGraphicsResourceSetMapFlags_v2 = NULL (empty)

478cdef void* __cuGraphicsMapResources = NULL (empty)

479cdef void* __cuGraphicsUnmapResources = NULL (empty)

480cdef void* __cuGetProcAddress_v2 = NULL (empty)

481cdef void* __cuCoredumpGetAttribute = NULL (empty)

482cdef void* __cuCoredumpGetAttributeGlobal = NULL (empty)

483cdef void* __cuCoredumpSetAttribute = NULL (empty)

484cdef void* __cuCoredumpSetAttributeGlobal = NULL (empty)

485cdef void* __cuGetExportTable = NULL (empty)

486cdef void* __cuGreenCtxCreate = NULL (empty)

487cdef void* __cuGreenCtxDestroy = NULL (empty)

488cdef void* __cuCtxFromGreenCtx = NULL (empty)

489cdef void* __cuDeviceGetDevResource = NULL (empty)

490cdef void* __cuCtxGetDevResource = NULL (empty)

491cdef void* __cuGreenCtxGetDevResource = NULL (empty)

492cdef void* __cuDevSmResourceSplitByCount = NULL (empty)

493cdef void* __cuDevResourceGenerateDesc = NULL (empty)

494cdef void* __cuGreenCtxRecordEvent = NULL (empty)

495cdef void* __cuGreenCtxWaitEvent = NULL (empty)

496cdef void* __cuStreamGetGreenCtx = NULL (empty)

497cdef void* __cuGreenCtxStreamCreate = NULL (empty)

498cdef void* __cuLogsRegisterCallback = NULL (empty)

499cdef void* __cuLogsUnregisterCallback = NULL (empty)

500cdef void* __cuLogsCurrent = NULL (empty)

501cdef void* __cuLogsDumpToFile = NULL (empty)

502cdef void* __cuLogsDumpToMemory = NULL (empty)

503cdef void* __cuCheckpointProcessGetRestoreThreadId = NULL (empty)

504cdef void* __cuCheckpointProcessGetState = NULL (empty)

505cdef void* __cuCheckpointProcessLock = NULL (empty)

506cdef void* __cuCheckpointProcessCheckpoint = NULL (empty)

507cdef void* __cuCheckpointProcessRestore = NULL (empty)

508cdef void* __cuCheckpointProcessUnlock = NULL (empty)

509cdef void* __cuGraphicsEGLRegisterImage = NULL (empty)

510cdef void* __cuEGLStreamConsumerConnect = NULL (empty)

511cdef void* __cuEGLStreamConsumerConnectWithFlags = NULL (empty)

512cdef void* __cuEGLStreamConsumerDisconnect = NULL (empty)

513cdef void* __cuEGLStreamConsumerAcquireFrame = NULL (empty)

514cdef void* __cuEGLStreamConsumerReleaseFrame = NULL (empty)

515cdef void* __cuEGLStreamProducerConnect = NULL (empty)

516cdef void* __cuEGLStreamProducerDisconnect = NULL (empty)

517cdef void* __cuEGLStreamProducerPresentFrame = NULL (empty)

518cdef void* __cuEGLStreamProducerReturnFrame = NULL (empty)

519cdef void* __cuGraphicsResourceGetMappedEglFrame = NULL (empty)

520cdef void* __cuEventCreateFromEGLSync = NULL (empty)

521cdef void* __cuGraphicsGLRegisterBuffer = NULL (empty)

522cdef void* __cuGraphicsGLRegisterImage = NULL (empty)

523cdef void* __cuGLGetDevices_v2 = NULL (empty)

524cdef void* __cuGLCtxCreate_v2 = NULL (empty)

525cdef void* __cuGLInit = NULL (empty)

526cdef void* __cuGLRegisterBufferObject = NULL (empty)

527cdef void* __cuGLMapBufferObject_v2 = NULL (empty)

528cdef void* __cuGLUnmapBufferObject = NULL (empty)

529cdef void* __cuGLUnregisterBufferObject = NULL (empty)

530cdef void* __cuGLSetBufferObjectMapFlags = NULL (empty)

531cdef void* __cuGLMapBufferObjectAsync_v2 = NULL (empty)

532cdef void* __cuGLUnmapBufferObjectAsync = NULL (empty)

533cdef void* __cuProfilerInitialize = NULL (empty)

534cdef void* __cuProfilerStart = NULL (empty)

535cdef void* __cuProfilerStop = NULL (empty)

536cdef void* __cuVDPAUGetDevice = NULL (empty)

537cdef void* __cuVDPAUCtxCreate_v2 = NULL (empty)

538cdef void* __cuGraphicsVDPAURegisterVideoSurface = NULL (empty)

539cdef void* __cuGraphicsVDPAURegisterOutputSurface = NULL (empty)

540cdef void* __cuDeviceGetHostAtomicCapabilities = NULL (empty)

541cdef void* __cuCtxGetDevice_v2 = NULL (empty)

542cdef void* __cuCtxSynchronize_v2 = NULL (empty)

543cdef void* __cuMemcpyBatchAsync_v2 = NULL (empty)

544cdef void* __cuMemcpy3DBatchAsync_v2 = NULL (empty)

545cdef void* __cuMemGetDefaultMemPool = NULL (empty)

546cdef void* __cuMemGetMemPool = NULL (empty)

547cdef void* __cuMemSetMemPool = NULL (empty)

548cdef void* __cuMemPrefetchBatchAsync = NULL (empty)

549cdef void* __cuMemDiscardBatchAsync = NULL (empty)

550cdef void* __cuMemDiscardAndPrefetchBatchAsync = NULL (empty)

551cdef void* __cuDeviceGetP2PAtomicCapabilities = NULL (empty)

552cdef void* __cuGreenCtxGetId = NULL (empty)

553cdef void* __cuMulticastBindMem_v2 = NULL (empty)

554cdef void* __cuMulticastBindAddr_v2 = NULL (empty)

555cdef void* __cuGraphNodeGetContainingGraph = NULL (empty)

556cdef void* __cuGraphNodeGetLocalId = NULL (empty)

557cdef void* __cuGraphNodeGetToolsId = NULL (empty)

558cdef void* __cuGraphGetId = NULL (empty)

559cdef void* __cuGraphExecGetId = NULL (empty)

560cdef void* __cuDevSmResourceSplit = NULL (empty)

561cdef void* __cuStreamGetDevResource = NULL (empty)

562cdef void* __cuKernelGetParamCount = NULL (empty)

563cdef void* __cuMemcpyWithAttributesAsync = NULL (empty)

564cdef void* __cuMemcpy3DWithAttributesAsync = NULL (empty)

565cdef void* __cuStreamBeginCaptureToCig = NULL (empty)

566cdef void* __cuStreamEndCaptureToCig = NULL (empty)

567cdef void* __cuFuncGetParamCount = NULL (empty)

568cdef void* __cuLaunchHostFunc_v2 = NULL (empty)

569cdef void* __cuGraphNodeGetParams = NULL (empty)

570cdef void* __cuCoredumpRegisterStartCallback = NULL (empty)

571cdef void* __cuCoredumpRegisterCompleteCallback = NULL (empty)

572cdef void* __cuCoredumpDeregisterStartCallback = NULL (empty)

573cdef void* __cuCoredumpDeregisterCompleteCallback = NULL (empty)

574cdef void* __cuLogicalEndpointIdReserve = NULL (empty)

575cdef void* __cuLogicalEndpointIdRelease = NULL (empty)

576cdef void* __cuLogicalEndpointCreate = NULL (empty)

577cdef void* __cuLogicalEndpointAddDevice = NULL (empty)

578cdef void* __cuLogicalEndpointDestroy = NULL (empty)

579cdef void* __cuLogicalEndpointBindAddr = NULL (empty)

580cdef void* __cuLogicalEndpointBindMem = NULL (empty)

581cdef void* __cuLogicalEndpointUnbind = NULL (empty)

582cdef void* __cuLogicalEndpointExport = NULL (empty)

583cdef void* __cuLogicalEndpointImport = NULL (empty)

584cdef void* __cuLogicalEndpointGetLimits = NULL (empty)

585cdef void* __cuLogicalEndpointQuery = NULL (empty)

586cdef void* __cuStreamBeginRecaptureToGraph = NULL (empty)

587cdef void* __cuDeviceGetFabricClusterUuid = NULL (empty)

588cdef void* __cuDeviceGetCliqueCount = NULL (empty)

589cdef void* __cuDeviceGetCliqueInfo = NULL (empty)

590cdef void* __cuMemGetLocationInfo = NULL (empty)

591cdef void* __cuGraphAddNode_v3 = NULL (empty)

592cdef void* __cuGraphNodeSetParams_v2 = NULL (empty)

593cdef void* __cuCheckpointOperationComplete = NULL (empty)

594  

595cdef int _init_driver() except -1 nogil: (empty)

596 global _cyb___py_driver_init 

597 cdef void* handle = NULL (empty)

598 cdef int ptds_mode 

599 cdef _cyb_cuGetProcAddress_v2_T cuGetProcAddress_v2 

600 with gil, _cyb_symbol_lock: (empty)

601 if _cyb___py_driver_init: return 0 (empty)

602  

603 handle = load_library() (empty)

604 if handle == NULL: (empty)

605 raise RuntimeError('Failed to open cuda') (empty)

606 # Get latest cuGetProcAddress_v2 

607 cuGetProcAddress_v2 = <_cyb_cuGetProcAddress_v2_T>_cyb_dlsym(handle, 'cuGetProcAddress_v2') (empty)

608 if cuGetProcAddress_v2 == NULL: (empty)

609 raise RuntimeError("Failed to get cuGetProcAddress_v2") 

610 if bool(int(_cyb_getenv('CUDA_PYTHON_CUDA_PER_THREAD_DEFAULT_STREAM', default=0))): (empty)

611 ptds_mode = CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM (empty)

612 else: 

613 ptds_mode = CU_GET_PROC_ADDRESS_DEFAULT (empty)

614 global __cuGetErrorString 

615 cuGetProcAddress_v2('cuGetErrorString', <void **>&__cuGetErrorString, 6000, ptds_mode, NULL) (empty)

616  

617 global __cuGetErrorName 

618 cuGetProcAddress_v2('cuGetErrorName', <void **>&__cuGetErrorName, 6000, ptds_mode, NULL) (empty)

619  

620 global __cuInit 

621 cuGetProcAddress_v2('cuInit', <void **>&__cuInit, 2000, ptds_mode, NULL) (empty)

622  

623 global __cuDriverGetVersion 

624 cuGetProcAddress_v2('cuDriverGetVersion', <void **>&__cuDriverGetVersion, 2020, ptds_mode, NULL) (empty)

625  

626 global __cuDeviceGet 

627 cuGetProcAddress_v2('cuDeviceGet', <void **>&__cuDeviceGet, 2000, ptds_mode, NULL) (empty)

628  

629 global __cuDeviceGetCount 

630 cuGetProcAddress_v2('cuDeviceGetCount', <void **>&__cuDeviceGetCount, 2000, ptds_mode, NULL) (empty)

631  

632 global __cuDeviceGetName 

633 cuGetProcAddress_v2('cuDeviceGetName', <void **>&__cuDeviceGetName, 2000, ptds_mode, NULL) (empty)

634  

635 global __cuDeviceGetUuid_v2 

636 cuGetProcAddress_v2('cuDeviceGetUuid', <void **>&__cuDeviceGetUuid_v2, 11040, ptds_mode, NULL) (empty)

637  

638 global __cuDeviceGetLuid 

639 cuGetProcAddress_v2('cuDeviceGetLuid', <void **>&__cuDeviceGetLuid, 10000, ptds_mode, NULL) (empty)

640  

641 global __cuDeviceTotalMem_v2 

642 cuGetProcAddress_v2('cuDeviceTotalMem', <void **>&__cuDeviceTotalMem_v2, 3020, ptds_mode, NULL) (empty)

643  

644 global __cuDeviceGetTexture1DLinearMaxWidth 

645 cuGetProcAddress_v2('cuDeviceGetTexture1DLinearMaxWidth', <void **>&__cuDeviceGetTexture1DLinearMaxWidth, 11010, ptds_mode, NULL) (empty)

646  

647 global __cuDeviceGetAttribute 

648 cuGetProcAddress_v2('cuDeviceGetAttribute', <void **>&__cuDeviceGetAttribute, 2000, ptds_mode, NULL) (empty)

649  

650 global __cuDeviceGetNvSciSyncAttributes 

651 cuGetProcAddress_v2('cuDeviceGetNvSciSyncAttributes', <void **>&__cuDeviceGetNvSciSyncAttributes, 10020, ptds_mode, NULL) (empty)

652  

653 global __cuDeviceSetMemPool 

654 cuGetProcAddress_v2('cuDeviceSetMemPool', <void **>&__cuDeviceSetMemPool, 11020, ptds_mode, NULL) (empty)

655  

656 global __cuDeviceGetMemPool 

657 cuGetProcAddress_v2('cuDeviceGetMemPool', <void **>&__cuDeviceGetMemPool, 11020, ptds_mode, NULL) (empty)

658  

659 global __cuDeviceGetDefaultMemPool 

660 cuGetProcAddress_v2('cuDeviceGetDefaultMemPool', <void **>&__cuDeviceGetDefaultMemPool, 11020, ptds_mode, NULL) (empty)

661  

662 global __cuDeviceGetExecAffinitySupport 

663 cuGetProcAddress_v2('cuDeviceGetExecAffinitySupport', <void **>&__cuDeviceGetExecAffinitySupport, 11040, ptds_mode, NULL) (empty)

664  

665 global __cuFlushGPUDirectRDMAWrites 

666 cuGetProcAddress_v2('cuFlushGPUDirectRDMAWrites', <void **>&__cuFlushGPUDirectRDMAWrites, 11030, ptds_mode, NULL) (empty)

667  

668 global __cuDeviceGetProperties 

669 cuGetProcAddress_v2('cuDeviceGetProperties', <void **>&__cuDeviceGetProperties, 2000, ptds_mode, NULL) (empty)

670  

671 global __cuDeviceComputeCapability 

672 cuGetProcAddress_v2('cuDeviceComputeCapability', <void **>&__cuDeviceComputeCapability, 2000, ptds_mode, NULL) (empty)

673  

674 global __cuDevicePrimaryCtxRetain 

675 cuGetProcAddress_v2('cuDevicePrimaryCtxRetain', <void **>&__cuDevicePrimaryCtxRetain, 7000, ptds_mode, NULL) (empty)

676  

677 global __cuDevicePrimaryCtxRelease_v2 

678 cuGetProcAddress_v2('cuDevicePrimaryCtxRelease', <void **>&__cuDevicePrimaryCtxRelease_v2, 11000, ptds_mode, NULL) (empty)

679  

680 global __cuDevicePrimaryCtxSetFlags_v2 

681 cuGetProcAddress_v2('cuDevicePrimaryCtxSetFlags', <void **>&__cuDevicePrimaryCtxSetFlags_v2, 11000, ptds_mode, NULL) (empty)

682  

683 global __cuDevicePrimaryCtxGetState 

684 cuGetProcAddress_v2('cuDevicePrimaryCtxGetState', <void **>&__cuDevicePrimaryCtxGetState, 7000, ptds_mode, NULL) (empty)

685  

686 global __cuDevicePrimaryCtxReset_v2 

687 cuGetProcAddress_v2('cuDevicePrimaryCtxReset', <void **>&__cuDevicePrimaryCtxReset_v2, 11000, ptds_mode, NULL) (empty)

688  

689 global __cuCtxCreate_v2 

690 cuGetProcAddress_v2('cuCtxCreate', <void **>&__cuCtxCreate_v2, 3020, ptds_mode, NULL) (empty)

691  

692 global __cuCtxCreate_v3 

693 cuGetProcAddress_v2('cuCtxCreate', <void **>&__cuCtxCreate_v3, 11040, ptds_mode, NULL) (empty)

694  

695 global __cuCtxCreate_v4 

696 cuGetProcAddress_v2('cuCtxCreate', <void **>&__cuCtxCreate_v4, 12050, ptds_mode, NULL) (empty)

697  

698 global __cuCtxDestroy_v2 

699 cuGetProcAddress_v2('cuCtxDestroy', <void **>&__cuCtxDestroy_v2, 4000, ptds_mode, NULL) (empty)

700  

701 global __cuCtxPushCurrent_v2 

702 cuGetProcAddress_v2('cuCtxPushCurrent', <void **>&__cuCtxPushCurrent_v2, 4000, ptds_mode, NULL) (empty)

703  

704 global __cuCtxPopCurrent_v2 

705 cuGetProcAddress_v2('cuCtxPopCurrent', <void **>&__cuCtxPopCurrent_v2, 4000, ptds_mode, NULL) (empty)

706  

707 global __cuCtxSetCurrent 

708 cuGetProcAddress_v2('cuCtxSetCurrent', <void **>&__cuCtxSetCurrent, 4000, ptds_mode, NULL) (empty)

709  

710 global __cuCtxGetCurrent 

711 cuGetProcAddress_v2('cuCtxGetCurrent', <void **>&__cuCtxGetCurrent, 4000, ptds_mode, NULL) (empty)

712  

713 global __cuCtxGetDevice 

714 cuGetProcAddress_v2('cuCtxGetDevice', <void **>&__cuCtxGetDevice, 2000, ptds_mode, NULL) (empty)

715  

716 global __cuCtxGetFlags 

717 cuGetProcAddress_v2('cuCtxGetFlags', <void **>&__cuCtxGetFlags, 7000, ptds_mode, NULL) (empty)

718  

719 global __cuCtxSetFlags 

720 cuGetProcAddress_v2('cuCtxSetFlags', <void **>&__cuCtxSetFlags, 12010, ptds_mode, NULL) (empty)

721  

722 global __cuCtxGetId 

723 cuGetProcAddress_v2('cuCtxGetId', <void **>&__cuCtxGetId, 12000, ptds_mode, NULL) (empty)

724  

725 global __cuCtxSynchronize 

726 cuGetProcAddress_v2('cuCtxSynchronize', <void **>&__cuCtxSynchronize, 2000, ptds_mode, NULL) (empty)

727  

728 global __cuCtxSetLimit 

729 cuGetProcAddress_v2('cuCtxSetLimit', <void **>&__cuCtxSetLimit, 3010, ptds_mode, NULL) (empty)

730  

731 global __cuCtxGetLimit 

732 cuGetProcAddress_v2('cuCtxGetLimit', <void **>&__cuCtxGetLimit, 3010, ptds_mode, NULL) (empty)

733  

734 global __cuCtxGetCacheConfig 

735 cuGetProcAddress_v2('cuCtxGetCacheConfig', <void **>&__cuCtxGetCacheConfig, 3020, ptds_mode, NULL) (empty)

736  

737 global __cuCtxSetCacheConfig 

738 cuGetProcAddress_v2('cuCtxSetCacheConfig', <void **>&__cuCtxSetCacheConfig, 3020, ptds_mode, NULL) (empty)

739  

740 global __cuCtxGetApiVersion 

741 cuGetProcAddress_v2('cuCtxGetApiVersion', <void **>&__cuCtxGetApiVersion, 3020, ptds_mode, NULL) (empty)

742  

743 global __cuCtxGetStreamPriorityRange 

744 cuGetProcAddress_v2('cuCtxGetStreamPriorityRange', <void **>&__cuCtxGetStreamPriorityRange, 5050, ptds_mode, NULL) (empty)

745  

746 global __cuCtxResetPersistingL2Cache 

747 cuGetProcAddress_v2('cuCtxResetPersistingL2Cache', <void **>&__cuCtxResetPersistingL2Cache, 11000, ptds_mode, NULL) (empty)

748  

749 global __cuCtxGetExecAffinity 

750 cuGetProcAddress_v2('cuCtxGetExecAffinity', <void **>&__cuCtxGetExecAffinity, 11040, ptds_mode, NULL) (empty)

751  

752 global __cuCtxRecordEvent 

753 cuGetProcAddress_v2('cuCtxRecordEvent', <void **>&__cuCtxRecordEvent, 12050, ptds_mode, NULL) (empty)

754  

755 global __cuCtxWaitEvent 

756 cuGetProcAddress_v2('cuCtxWaitEvent', <void **>&__cuCtxWaitEvent, 12050, ptds_mode, NULL) (empty)

757  

758 global __cuCtxAttach 

759 cuGetProcAddress_v2('cuCtxAttach', <void **>&__cuCtxAttach, 2000, ptds_mode, NULL) (empty)

760  

761 global __cuCtxDetach 

762 cuGetProcAddress_v2('cuCtxDetach', <void **>&__cuCtxDetach, 2000, ptds_mode, NULL) (empty)

763  

764 global __cuCtxGetSharedMemConfig 

765 cuGetProcAddress_v2('cuCtxGetSharedMemConfig', <void **>&__cuCtxGetSharedMemConfig, 4020, ptds_mode, NULL) (empty)

766  

767 global __cuCtxSetSharedMemConfig 

768 cuGetProcAddress_v2('cuCtxSetSharedMemConfig', <void **>&__cuCtxSetSharedMemConfig, 4020, ptds_mode, NULL) (empty)

769  

770 global __cuModuleLoad 

771 cuGetProcAddress_v2('cuModuleLoad', <void **>&__cuModuleLoad, 2000, ptds_mode, NULL) (empty)

772  

773 global __cuModuleLoadData 

774 cuGetProcAddress_v2('cuModuleLoadData', <void **>&__cuModuleLoadData, 2000, ptds_mode, NULL) (empty)

775  

776 global __cuModuleLoadDataEx 

777 cuGetProcAddress_v2('cuModuleLoadDataEx', <void **>&__cuModuleLoadDataEx, 2010, ptds_mode, NULL) (empty)

778  

779 global __cuModuleLoadFatBinary 

780 cuGetProcAddress_v2('cuModuleLoadFatBinary', <void **>&__cuModuleLoadFatBinary, 2000, ptds_mode, NULL) (empty)

781  

782 global __cuModuleUnload 

783 cuGetProcAddress_v2('cuModuleUnload', <void **>&__cuModuleUnload, 2000, ptds_mode, NULL) (empty)

784  

785 global __cuModuleGetLoadingMode 

786 cuGetProcAddress_v2('cuModuleGetLoadingMode', <void **>&__cuModuleGetLoadingMode, 11070, ptds_mode, NULL) (empty)

787  

788 global __cuModuleGetFunction 

789 cuGetProcAddress_v2('cuModuleGetFunction', <void **>&__cuModuleGetFunction, 2000, ptds_mode, NULL) (empty)

790  

791 global __cuModuleGetFunctionCount 

792 cuGetProcAddress_v2('cuModuleGetFunctionCount', <void **>&__cuModuleGetFunctionCount, 12040, ptds_mode, NULL) (empty)

793  

794 global __cuModuleEnumerateFunctions 

795 cuGetProcAddress_v2('cuModuleEnumerateFunctions', <void **>&__cuModuleEnumerateFunctions, 12040, ptds_mode, NULL) (empty)

796  

797 global __cuModuleGetGlobal_v2 

798 cuGetProcAddress_v2('cuModuleGetGlobal', <void **>&__cuModuleGetGlobal_v2, 3020, ptds_mode, NULL) (empty)

799  

800 global __cuLinkCreate_v2 

801 cuGetProcAddress_v2('cuLinkCreate', <void **>&__cuLinkCreate_v2, 6050, ptds_mode, NULL) (empty)

802  

803 global __cuLinkAddData_v2 

804 cuGetProcAddress_v2('cuLinkAddData', <void **>&__cuLinkAddData_v2, 6050, ptds_mode, NULL) (empty)

805  

806 global __cuLinkAddFile_v2 

807 cuGetProcAddress_v2('cuLinkAddFile', <void **>&__cuLinkAddFile_v2, 6050, ptds_mode, NULL) (empty)

808  

809 global __cuLinkComplete 

810 cuGetProcAddress_v2('cuLinkComplete', <void **>&__cuLinkComplete, 5050, ptds_mode, NULL) (empty)

811  

812 global __cuLinkDestroy 

813 cuGetProcAddress_v2('cuLinkDestroy', <void **>&__cuLinkDestroy, 5050, ptds_mode, NULL) (empty)

814  

815 global __cuModuleGetTexRef 

816 cuGetProcAddress_v2('cuModuleGetTexRef', <void **>&__cuModuleGetTexRef, 2000, ptds_mode, NULL) (empty)

817  

818 global __cuModuleGetSurfRef 

819 cuGetProcAddress_v2('cuModuleGetSurfRef', <void **>&__cuModuleGetSurfRef, 3000, ptds_mode, NULL) (empty)

820  

821 global __cuLibraryLoadData 

822 cuGetProcAddress_v2('cuLibraryLoadData', <void **>&__cuLibraryLoadData, 12000, ptds_mode, NULL) (empty)

823  

824 global __cuLibraryLoadFromFile 

825 cuGetProcAddress_v2('cuLibraryLoadFromFile', <void **>&__cuLibraryLoadFromFile, 12000, ptds_mode, NULL) (empty)

826  

827 global __cuLibraryUnload 

828 cuGetProcAddress_v2('cuLibraryUnload', <void **>&__cuLibraryUnload, 12000, ptds_mode, NULL) (empty)

829  

830 global __cuLibraryGetKernel 

831 cuGetProcAddress_v2('cuLibraryGetKernel', <void **>&__cuLibraryGetKernel, 12000, ptds_mode, NULL) (empty)

832  

833 global __cuLibraryGetKernelCount 

834 cuGetProcAddress_v2('cuLibraryGetKernelCount', <void **>&__cuLibraryGetKernelCount, 12040, ptds_mode, NULL) (empty)

835  

836 global __cuLibraryEnumerateKernels 

837 cuGetProcAddress_v2('cuLibraryEnumerateKernels', <void **>&__cuLibraryEnumerateKernels, 12040, ptds_mode, NULL) (empty)

838  

839 global __cuLibraryGetModule 

840 cuGetProcAddress_v2('cuLibraryGetModule', <void **>&__cuLibraryGetModule, 12000, ptds_mode, NULL) (empty)

841  

842 global __cuKernelGetFunction 

843 cuGetProcAddress_v2('cuKernelGetFunction', <void **>&__cuKernelGetFunction, 12000, ptds_mode, NULL) (empty)

844  

845 global __cuKernelGetLibrary 

846 cuGetProcAddress_v2('cuKernelGetLibrary', <void **>&__cuKernelGetLibrary, 12050, ptds_mode, NULL) (empty)

847  

848 global __cuLibraryGetGlobal 

849 cuGetProcAddress_v2('cuLibraryGetGlobal', <void **>&__cuLibraryGetGlobal, 12000, ptds_mode, NULL) (empty)

850  

851 global __cuLibraryGetManaged 

852 cuGetProcAddress_v2('cuLibraryGetManaged', <void **>&__cuLibraryGetManaged, 12000, ptds_mode, NULL) (empty)

853  

854 global __cuLibraryGetUnifiedFunction 

855 cuGetProcAddress_v2('cuLibraryGetUnifiedFunction', <void **>&__cuLibraryGetUnifiedFunction, 12000, ptds_mode, NULL) (empty)

856  

857 global __cuKernelGetAttribute 

858 cuGetProcAddress_v2('cuKernelGetAttribute', <void **>&__cuKernelGetAttribute, 12000, ptds_mode, NULL) (empty)

859  

860 global __cuKernelSetAttribute 

861 cuGetProcAddress_v2('cuKernelSetAttribute', <void **>&__cuKernelSetAttribute, 12000, ptds_mode, NULL) (empty)

862  

863 global __cuKernelSetCacheConfig 

864 cuGetProcAddress_v2('cuKernelSetCacheConfig', <void **>&__cuKernelSetCacheConfig, 12000, ptds_mode, NULL) (empty)

865  

866 global __cuKernelGetName 

867 cuGetProcAddress_v2('cuKernelGetName', <void **>&__cuKernelGetName, 12030, ptds_mode, NULL) (empty)

868  

869 global __cuKernelGetParamInfo 

870 cuGetProcAddress_v2('cuKernelGetParamInfo', <void **>&__cuKernelGetParamInfo, 12040, ptds_mode, NULL) (empty)

871  

872 global __cuMemGetInfo_v2 

873 cuGetProcAddress_v2('cuMemGetInfo', <void **>&__cuMemGetInfo_v2, 3020, ptds_mode, NULL) (empty)

874  

875 global __cuMemAlloc_v2 

876 cuGetProcAddress_v2('cuMemAlloc', <void **>&__cuMemAlloc_v2, 3020, ptds_mode, NULL) (empty)

877  

878 global __cuMemAllocPitch_v2 

879 cuGetProcAddress_v2('cuMemAllocPitch', <void **>&__cuMemAllocPitch_v2, 3020, ptds_mode, NULL) (empty)

880  

881 global __cuMemFree_v2 

882 cuGetProcAddress_v2('cuMemFree', <void **>&__cuMemFree_v2, 3020, ptds_mode, NULL) (empty)

883  

884 global __cuMemGetAddressRange_v2 

885 cuGetProcAddress_v2('cuMemGetAddressRange', <void **>&__cuMemGetAddressRange_v2, 3020, ptds_mode, NULL) (empty)

886  

887 global __cuMemAllocHost_v2 

888 cuGetProcAddress_v2('cuMemAllocHost', <void **>&__cuMemAllocHost_v2, 3020, ptds_mode, NULL) (empty)

889  

890 global __cuMemFreeHost 

891 cuGetProcAddress_v2('cuMemFreeHost', <void **>&__cuMemFreeHost, 2000, ptds_mode, NULL) (empty)

892  

893 global __cuMemHostAlloc 

894 cuGetProcAddress_v2('cuMemHostAlloc', <void **>&__cuMemHostAlloc, 2020, ptds_mode, NULL) (empty)

895  

896 global __cuMemHostGetDevicePointer_v2 

897 cuGetProcAddress_v2('cuMemHostGetDevicePointer', <void **>&__cuMemHostGetDevicePointer_v2, 3020, ptds_mode, NULL) (empty)

898  

899 global __cuMemHostGetFlags 

900 cuGetProcAddress_v2('cuMemHostGetFlags', <void **>&__cuMemHostGetFlags, 2030, ptds_mode, NULL) (empty)

901  

902 global __cuMemAllocManaged 

903 cuGetProcAddress_v2('cuMemAllocManaged', <void **>&__cuMemAllocManaged, 6000, ptds_mode, NULL) (empty)

904  

905 global __cuDeviceRegisterAsyncNotification 

906 cuGetProcAddress_v2('cuDeviceRegisterAsyncNotification', <void **>&__cuDeviceRegisterAsyncNotification, 12040, ptds_mode, NULL) (empty)

907  

908 global __cuDeviceUnregisterAsyncNotification 

909 cuGetProcAddress_v2('cuDeviceUnregisterAsyncNotification', <void **>&__cuDeviceUnregisterAsyncNotification, 12040, ptds_mode, NULL) (empty)

910  

911 global __cuDeviceGetByPCIBusId 

912 cuGetProcAddress_v2('cuDeviceGetByPCIBusId', <void **>&__cuDeviceGetByPCIBusId, 4010, ptds_mode, NULL) (empty)

913  

914 global __cuDeviceGetPCIBusId 

915 cuGetProcAddress_v2('cuDeviceGetPCIBusId', <void **>&__cuDeviceGetPCIBusId, 4010, ptds_mode, NULL) (empty)

916  

917 global __cuIpcGetEventHandle 

918 cuGetProcAddress_v2('cuIpcGetEventHandle', <void **>&__cuIpcGetEventHandle, 4010, ptds_mode, NULL) (empty)

919  

920 global __cuIpcOpenEventHandle 

921 cuGetProcAddress_v2('cuIpcOpenEventHandle', <void **>&__cuIpcOpenEventHandle, 4010, ptds_mode, NULL) (empty)

922  

923 global __cuIpcGetMemHandle 

924 cuGetProcAddress_v2('cuIpcGetMemHandle', <void **>&__cuIpcGetMemHandle, 4010, ptds_mode, NULL) (empty)

925  

926 global __cuIpcOpenMemHandle_v2 

927 cuGetProcAddress_v2('cuIpcOpenMemHandle', <void **>&__cuIpcOpenMemHandle_v2, 11000, ptds_mode, NULL) (empty)

928  

929 global __cuIpcCloseMemHandle 

930 cuGetProcAddress_v2('cuIpcCloseMemHandle', <void **>&__cuIpcCloseMemHandle, 4010, ptds_mode, NULL) (empty)

931  

932 global __cuMemHostRegister_v2 

933 cuGetProcAddress_v2('cuMemHostRegister', <void **>&__cuMemHostRegister_v2, 6050, ptds_mode, NULL) (empty)

934  

935 global __cuMemHostUnregister 

936 cuGetProcAddress_v2('cuMemHostUnregister', <void **>&__cuMemHostUnregister, 4000, ptds_mode, NULL) (empty)

937  

938 global __cuMemcpy 

939 cuGetProcAddress_v2('cuMemcpy', <void **>&__cuMemcpy, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 4000, ptds_mode, NULL) (empty)

940  

941 global __cuMemcpyPeer 

942 cuGetProcAddress_v2('cuMemcpyPeer', <void **>&__cuMemcpyPeer, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 4000, ptds_mode, NULL) (empty)

943  

944 global __cuMemcpyHtoD_v2 

945 cuGetProcAddress_v2('cuMemcpyHtoD', <void **>&__cuMemcpyHtoD_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

946  

947 global __cuMemcpyDtoH_v2 

948 cuGetProcAddress_v2('cuMemcpyDtoH', <void **>&__cuMemcpyDtoH_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

949  

950 global __cuMemcpyDtoD_v2 

951 cuGetProcAddress_v2('cuMemcpyDtoD', <void **>&__cuMemcpyDtoD_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

952  

953 global __cuMemcpyDtoA_v2 

954 cuGetProcAddress_v2('cuMemcpyDtoA', <void **>&__cuMemcpyDtoA_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

955  

956 global __cuMemcpyAtoD_v2 

957 cuGetProcAddress_v2('cuMemcpyAtoD', <void **>&__cuMemcpyAtoD_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

958  

959 global __cuMemcpyHtoA_v2 

960 cuGetProcAddress_v2('cuMemcpyHtoA', <void **>&__cuMemcpyHtoA_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

961  

962 global __cuMemcpyAtoH_v2 

963 cuGetProcAddress_v2('cuMemcpyAtoH', <void **>&__cuMemcpyAtoH_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

964  

965 global __cuMemcpyAtoA_v2 

966 cuGetProcAddress_v2('cuMemcpyAtoA', <void **>&__cuMemcpyAtoA_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

967  

968 global __cuMemcpy2D_v2 

969 cuGetProcAddress_v2('cuMemcpy2D', <void **>&__cuMemcpy2D_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

970  

971 global __cuMemcpy2DUnaligned_v2 

972 cuGetProcAddress_v2('cuMemcpy2DUnaligned', <void **>&__cuMemcpy2DUnaligned_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

973  

974 global __cuMemcpy3D_v2 

975 cuGetProcAddress_v2('cuMemcpy3D', <void **>&__cuMemcpy3D_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

976  

977 global __cuMemcpy3DPeer 

978 cuGetProcAddress_v2('cuMemcpy3DPeer', <void **>&__cuMemcpy3DPeer, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 4000, ptds_mode, NULL) (empty)

979  

980 global __cuMemcpyAsync 

981 cuGetProcAddress_v2('cuMemcpyAsync', <void **>&__cuMemcpyAsync, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 4000, ptds_mode, NULL) (empty)

982  

983 global __cuMemcpyPeerAsync 

984 cuGetProcAddress_v2('cuMemcpyPeerAsync', <void **>&__cuMemcpyPeerAsync, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 4000, ptds_mode, NULL) (empty)

985  

986 global __cuMemcpyHtoDAsync_v2 

987 cuGetProcAddress_v2('cuMemcpyHtoDAsync', <void **>&__cuMemcpyHtoDAsync_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

988  

989 global __cuMemcpyDtoHAsync_v2 

990 cuGetProcAddress_v2('cuMemcpyDtoHAsync', <void **>&__cuMemcpyDtoHAsync_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

991  

992 global __cuMemcpyDtoDAsync_v2 

993 cuGetProcAddress_v2('cuMemcpyDtoDAsync', <void **>&__cuMemcpyDtoDAsync_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

994  

995 global __cuMemcpyHtoAAsync_v2 

996 cuGetProcAddress_v2('cuMemcpyHtoAAsync', <void **>&__cuMemcpyHtoAAsync_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

997  

998 global __cuMemcpyAtoHAsync_v2 

999 cuGetProcAddress_v2('cuMemcpyAtoHAsync', <void **>&__cuMemcpyAtoHAsync_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1000  

1001 global __cuMemcpy2DAsync_v2 

1002 cuGetProcAddress_v2('cuMemcpy2DAsync', <void **>&__cuMemcpy2DAsync_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1003  

1004 global __cuMemcpy3DAsync_v2 

1005 cuGetProcAddress_v2('cuMemcpy3DAsync', <void **>&__cuMemcpy3DAsync_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1006  

1007 global __cuMemcpy3DPeerAsync 

1008 cuGetProcAddress_v2('cuMemcpy3DPeerAsync', <void **>&__cuMemcpy3DPeerAsync, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 4000, ptds_mode, NULL) (empty)

1009  

1010 global __cuMemsetD8_v2 

1011 cuGetProcAddress_v2('cuMemsetD8', <void **>&__cuMemsetD8_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1012  

1013 global __cuMemsetD16_v2 

1014 cuGetProcAddress_v2('cuMemsetD16', <void **>&__cuMemsetD16_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1015  

1016 global __cuMemsetD32_v2 

1017 cuGetProcAddress_v2('cuMemsetD32', <void **>&__cuMemsetD32_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1018  

1019 global __cuMemsetD2D8_v2 

1020 cuGetProcAddress_v2('cuMemsetD2D8', <void **>&__cuMemsetD2D8_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1021  

1022 global __cuMemsetD2D16_v2 

1023 cuGetProcAddress_v2('cuMemsetD2D16', <void **>&__cuMemsetD2D16_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1024  

1025 global __cuMemsetD2D32_v2 

1026 cuGetProcAddress_v2('cuMemsetD2D32', <void **>&__cuMemsetD2D32_v2, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1027  

1028 global __cuMemsetD8Async 

1029 cuGetProcAddress_v2('cuMemsetD8Async', <void **>&__cuMemsetD8Async, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1030  

1031 global __cuMemsetD16Async 

1032 cuGetProcAddress_v2('cuMemsetD16Async', <void **>&__cuMemsetD16Async, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1033  

1034 global __cuMemsetD32Async 

1035 cuGetProcAddress_v2('cuMemsetD32Async', <void **>&__cuMemsetD32Async, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1036  

1037 global __cuMemsetD2D8Async 

1038 cuGetProcAddress_v2('cuMemsetD2D8Async', <void **>&__cuMemsetD2D8Async, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1039  

1040 global __cuMemsetD2D16Async 

1041 cuGetProcAddress_v2('cuMemsetD2D16Async', <void **>&__cuMemsetD2D16Async, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1042  

1043 global __cuMemsetD2D32Async 

1044 cuGetProcAddress_v2('cuMemsetD2D32Async', <void **>&__cuMemsetD2D32Async, 7000 if ptds_mode == CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM else 3020, ptds_mode, NULL) (empty)

1045  

1046 global __cuArrayCreate_v2 

1047 cuGetProcAddress_v2('cuArrayCreate', <void **>&__cuArrayCreate_v2, 3020, ptds_mode, NULL) (empty)

1048  

1049 global __cuArrayGetDescriptor_v2 

1050 cuGetProcAddress_v2('cuArrayGetDescriptor', <void **>&__cuArrayGetDescriptor_v2, 3020, ptds_mode, NULL) (empty)

1051  

1052 global __cuArrayGetSparseProperties 

1053 cuGetProcAddress_v2('cuArrayGetSparseProperties', <void **>&__cuArrayGetSparseProperties, 11010, ptds_mode, NULL) (empty)

1054  

1055 global __cuMipmappedArrayGetSparseProperties 

1056 cuGetProcAddress_v2('cuMipmappedArrayGetSparseProperties', <void **>&__cuMipmappedArrayGetSparseProperties, 11010, ptds_mode, NULL) (empty)

1057  

1058 global __cuArrayGetMemoryRequirements 

1059 cuGetProcAddress_v2('cuArrayGetMemoryRequirements', <void **>&__cuArrayGetMemoryRequirements, 11060, ptds_mode, NULL) (empty)

1060  

1061 global __cuMipmappedArrayGetMemoryRequirements 

1062 cuGetProcAddress_v2('cuMipmappedArrayGetMemoryRequirements', <void **>&__cuMipmappedArrayGetMemoryRequirements, 11060, ptds_mode, NULL) (empty)

1063  

1064 global __cuArrayGetPlane 

1065 cuGetProcAddress_v2('cuArrayGetPlane', <void **>&__cuArrayGetPlane, 11020, ptds_mode, NULL) (empty)

1066  

1067 global __cuArrayDestroy 

1068 cuGetProcAddress_v2('cuArrayDestroy', <void **>&__cuArrayDestroy, 2000, ptds_mode, NULL) (empty)

1069  

1070 global __cuArray3DCreate_v2 

1071 cuGetProcAddress_v2('cuArray3DCreate', <void **>&__cuArray3DCreate_v2, 3020, ptds_mode, NULL) (empty)

1072  

1073 global __cuArray3DGetDescriptor_v2 

1074 cuGetProcAddress_v2('cuArray3DGetDescriptor', <void **>&__cuArray3DGetDescriptor_v2, 3020, ptds_mode, NULL) (empty)

1075  

1076 global __cuMipmappedArrayCreate 

1077 cuGetProcAddress_v2('cuMipmappedArrayCreate', <void **>&__cuMipmappedArrayCreate, 5000, ptds_mode, NULL) (empty)

1078  

1079 global __cuMipmappedArrayGetLevel 

1080 cuGetProcAddress_v2('cuMipmappedArrayGetLevel', <void **>&__cuMipmappedArrayGetLevel, 5000, ptds_mode, NULL) (empty)

1081  

1082 global __cuMipmappedArrayDestroy 

1083 cuGetProcAddress_v2('cuMipmappedArrayDestroy', <void **>&__cuMipmappedArrayDestroy, 5000, ptds_mode, NULL) (empty)

1084  

1085 global __cuMemGetHandleForAddressRange 

1086 cuGetProcAddress_v2('cuMemGetHandleForAddressRange', <void **>&__cuMemGetHandleForAddressRange, 11070, ptds_mode, NULL) (empty)

1087  

1088 global __cuMemBatchDecompressAsync 

1089 cuGetProcAddress_v2('cuMemBatchDecompressAsync', <void **>&__cuMemBatchDecompressAsync, 12060, ptds_mode, NULL) (empty)

1090  

1091 global __cuMemAddressReserve 

1092 cuGetProcAddress_v2('cuMemAddressReserve', <void **>&__cuMemAddressReserve, 10020, ptds_mode, NULL) (empty)

1093  

1094 global __cuMemAddressFree 

1095 cuGetProcAddress_v2('cuMemAddressFree', <void **>&__cuMemAddressFree, 10020, ptds_mode, NULL) (empty)

1096  

1097 global __cuMemCreate 

1098 cuGetProcAddress_v2('cuMemCreate', <void **>&__cuMemCreate, 10020, ptds_mode, NULL) (empty)

1099  

1100 global __cuMemRelease 

1101 cuGetProcAddress_v2('cuMemRelease', <void **>&__cuMemRelease, 10020, ptds_mode, NULL) (empty)

1102  

1103 global __cuMemMap 

1104 cuGetProcAddress_v2('cuMemMap', <void **>&__cuMemMap, 10020, ptds_mode, NULL) (empty)

1105  

1106 global __cuMemMapArrayAsync 

1107 cuGetProcAddress_v2('cuMemMapArrayAsync', <void **>&__cuMemMapArrayAsync, 11010, ptds_mode, NULL) (empty)

1108  

1109 global __cuMemUnmap 

1110 cuGetProcAddress_v2('cuMemUnmap', <void **>&__cuMemUnmap, 10020, ptds_mode, NULL) (empty)

1111  

1112 global __cuMemSetAccess 

1113 cuGetProcAddress_v2('cuMemSetAccess', <void **>&__cuMemSetAccess, 10020, ptds_mode, NULL) (empty)

1114  

1115 global __cuMemGetAccess 

1116 cuGetProcAddress_v2('cuMemGetAccess', <void **>&__cuMemGetAccess, 10020, ptds_mode, NULL) (empty)

1117  

1118 global __cuMemExportToShareableHandle 

1119 cuGetProcAddress_v2('cuMemExportToShareableHandle', <void **>&__cuMemExportToShareableHandle, 10020, ptds_mode, NULL) (empty)

1120  

1121 global __cuMemImportFromShareableHandle 

1122 cuGetProcAddress_v2('cuMemImportFromShareableHandle', <void **>&__cuMemImportFromShareableHandle, 10020, ptds_mode, NULL) (empty)

1123  

1124 global __cuMemGetAllocationGranularity 

1125 cuGetProcAddress_v2('cuMemGetAllocationGranularity', <void **>&__cuMemGetAllocationGranularity, 10020, ptds_mode, NULL) (empty)

1126  

1127 global __cuMemGetAllocationPropertiesFromHandle 

1128 cuGetProcAddress_v2('cuMemGetAllocationPropertiesFromHandle', <void **>&__cuMemGetAllocationPropertiesFromHandle, 10020, ptds_mode, NULL) (empty)

1129  

1130 global __cuMemRetainAllocationHandle 

1131 cuGetProcAddress_v2('cuMemRetainAllocationHandle', <void **>&__cuMemRetainAllocationHandle, 11000, ptds_mode, NULL) (empty)

1132  

1133 global __cuMemFreeAsync 

1134 cuGetProcAddress_v2('cuMemFreeAsync', <void **>&__cuMemFreeAsync, 11020, ptds_mode, NULL) (empty)

1135  

1136 global __cuMemAllocAsync 

1137 cuGetProcAddress_v2('cuMemAllocAsync', <void **>&__cuMemAllocAsync, 11020, ptds_mode, NULL) (empty)

1138  

1139 global __cuMemPoolTrimTo 

1140 cuGetProcAddress_v2('cuMemPoolTrimTo', <void **>&__cuMemPoolTrimTo, 11020, ptds_mode, NULL) (empty)

1141  

1142 global __cuMemPoolSetAttribute 

1143 cuGetProcAddress_v2('cuMemPoolSetAttribute', <void **>&__cuMemPoolSetAttribute, 11020, ptds_mode, NULL) (empty)

1144  

1145 global __cuMemPoolGetAttribute 

1146 cuGetProcAddress_v2('cuMemPoolGetAttribute', <void **>&__cuMemPoolGetAttribute, 11020, ptds_mode, NULL) (empty)

1147  

1148 global __cuMemPoolSetAccess 

1149 cuGetProcAddress_v2('cuMemPoolSetAccess', <void **>&__cuMemPoolSetAccess, 11020, ptds_mode, NULL) (empty)

1150  

1151 global __cuMemPoolGetAccess 

1152 cuGetProcAddress_v2('cuMemPoolGetAccess', <void **>&__cuMemPoolGetAccess, 11020, ptds_mode, NULL) (empty)

1153  

1154 global __cuMemPoolCreate 

1155 cuGetProcAddress_v2('cuMemPoolCreate', <void **>&__cuMemPoolCreate, 11020, ptds_mode, NULL) (empty)

1156  

1157 global __cuMemPoolDestroy 

1158 cuGetProcAddress_v2('cuMemPoolDestroy', <void **>&__cuMemPoolDestroy, 11020, ptds_mode, NULL) (empty)

1159  

1160 global __cuMemAllocFromPoolAsync 

1161 cuGetProcAddress_v2('cuMemAllocFromPoolAsync', <void **>&__cuMemAllocFromPoolAsync, 11020, ptds_mode, NULL) (empty)

1162  

1163 global __cuMemPoolExportToShareableHandle 

1164 cuGetProcAddress_v2('cuMemPoolExportToShareableHandle', <void **>&__cuMemPoolExportToShareableHandle, 11020, ptds_mode, NULL) (empty)

1165  

1166 global __cuMemPoolImportFromShareableHandle 

1167 cuGetProcAddress_v2('cuMemPoolImportFromShareableHandle', <void **>&__cuMemPoolImportFromShareableHandle, 11020, ptds_mode, NULL) (empty)

1168  

1169 global __cuMemPoolExportPointer 

1170 cuGetProcAddress_v2('cuMemPoolExportPointer', <void **>&__cuMemPoolExportPointer, 11020, ptds_mode, NULL) (empty)

1171  

1172 global __cuMemPoolImportPointer 

1173 cuGetProcAddress_v2('cuMemPoolImportPointer', <void **>&__cuMemPoolImportPointer, 11020, ptds_mode, NULL) (empty)

1174  

1175 global __cuMulticastCreate 

1176 cuGetProcAddress_v2('cuMulticastCreate', <void **>&__cuMulticastCreate, 12010, ptds_mode, NULL) (empty)

1177  

1178 global __cuMulticastAddDevice 

1179 cuGetProcAddress_v2('cuMulticastAddDevice', <void **>&__cuMulticastAddDevice, 12010, ptds_mode, NULL) (empty)

1180  

1181 global __cuMulticastBindMem 

1182 cuGetProcAddress_v2('cuMulticastBindMem', <void **>&__cuMulticastBindMem, 12010, ptds_mode, NULL) (empty)

1183  

1184 global __cuMulticastBindAddr 

1185 cuGetProcAddress_v2('cuMulticastBindAddr', <void **>&__cuMulticastBindAddr, 12010, ptds_mode, NULL) (empty)

1186  

1187 global __cuMulticastUnbind 

1188 cuGetProcAddress_v2('cuMulticastUnbind', <void **>&__cuMulticastUnbind, 12010, ptds_mode, NULL) (empty)

1189  

1190 global __cuMulticastGetGranularity 

1191 cuGetProcAddress_v2('cuMulticastGetGranularity', <void **>&__cuMulticastGetGranularity, 12010, ptds_mode, NULL) (empty)

1192  

1193 global __cuPointerGetAttribute 

1194 cuGetProcAddress_v2('cuPointerGetAttribute', <void **>&__cuPointerGetAttribute, 4000, ptds_mode, NULL) (empty)

1195  

1196 global __cuMemPrefetchAsync_v2 

1197 cuGetProcAddress_v2('cuMemPrefetchAsync', <void **>&__cuMemPrefetchAsync_v2, 12020, ptds_mode, NULL) (empty)

1198  

1199 global __cuMemAdvise_v2 

1200 cuGetProcAddress_v2('cuMemAdvise', <void **>&__cuMemAdvise_v2, 12020, ptds_mode, NULL) (empty)

1201  

1202 global __cuMemRangeGetAttribute 

1203 cuGetProcAddress_v2('cuMemRangeGetAttribute', <void **>&__cuMemRangeGetAttribute, 8000, ptds_mode, NULL) (empty)

1204  

1205 global __cuMemRangeGetAttributes 

1206 cuGetProcAddress_v2('cuMemRangeGetAttributes', <void **>&__cuMemRangeGetAttributes, 8000, ptds_mode, NULL) (empty)

1207  

1208 global __cuPointerSetAttribute 

1209 cuGetProcAddress_v2('cuPointerSetAttribute', <void **>&__cuPointerSetAttribute, 6000, ptds_mode, NULL) (empty)

1210