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

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.3.0. Do not modify it directly. 

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

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 as _cyb_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)

587  

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

589 global _cyb___py_driver_init 

590 cdef void* handle = NULL (empty)

591 cdef int ptds_mode 

592 cdef _cyb_cuGetProcAddress_v2_T cuGetProcAddress_v2 

593 with gil, _cyb_symbol_lock: (empty)

594 if _cyb___py_driver_init: return 0 (empty)

595  

596 handle = load_library() (empty)

597 if handle == NULL: (empty)

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

599 # Get latest cuGetProcAddress_v2 

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

601 if cuGetProcAddress_v2 == NULL: (empty)

602 raise RuntimeError("Failed to get cuGetProcAddress_v2") 

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

604 ptds_mode = CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM (empty)

605 else: 

606 ptds_mode = CU_GET_PROC_ADDRESS_DEFAULT (empty)

607 global __cuGetErrorString 

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

609  

610 global __cuGetErrorName 

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

612  

613 global __cuInit 

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

615  

616 global __cuDriverGetVersion 

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

618  

619 global __cuDeviceGet 

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

621  

622 global __cuDeviceGetCount 

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

624  

625 global __cuDeviceGetName 

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

627  

628 global __cuDeviceGetUuid_v2 

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

630  

631 global __cuDeviceGetLuid 

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

633  

634 global __cuDeviceTotalMem_v2 

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

636  

637 global __cuDeviceGetTexture1DLinearMaxWidth 

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

639  

640 global __cuDeviceGetAttribute 

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

642  

643 global __cuDeviceGetNvSciSyncAttributes 

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

645  

646 global __cuDeviceSetMemPool 

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

648  

649 global __cuDeviceGetMemPool 

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

651  

652 global __cuDeviceGetDefaultMemPool 

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

654  

655 global __cuDeviceGetExecAffinitySupport 

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

657  

658 global __cuFlushGPUDirectRDMAWrites 

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

660  

661 global __cuDeviceGetProperties 

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

663  

664 global __cuDeviceComputeCapability 

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

666  

667 global __cuDevicePrimaryCtxRetain 

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

669  

670 global __cuDevicePrimaryCtxRelease_v2 

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

672  

673 global __cuDevicePrimaryCtxSetFlags_v2 

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

675  

676 global __cuDevicePrimaryCtxGetState 

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

678  

679 global __cuDevicePrimaryCtxReset_v2 

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

681  

682 global __cuCtxCreate_v2 

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

684  

685 global __cuCtxCreate_v3 

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

687  

688 global __cuCtxCreate_v4 

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

690  

691 global __cuCtxDestroy_v2 

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

693  

694 global __cuCtxPushCurrent_v2 

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

696  

697 global __cuCtxPopCurrent_v2 

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

699  

700 global __cuCtxSetCurrent 

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

702  

703 global __cuCtxGetCurrent 

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

705  

706 global __cuCtxGetDevice 

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

708  

709 global __cuCtxGetFlags 

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

711  

712 global __cuCtxSetFlags 

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

714  

715 global __cuCtxGetId 

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

717  

718 global __cuCtxSynchronize 

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

720  

721 global __cuCtxSetLimit 

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

723  

724 global __cuCtxGetLimit 

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

726  

727 global __cuCtxGetCacheConfig 

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

729  

730 global __cuCtxSetCacheConfig 

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

732  

733 global __cuCtxGetApiVersion 

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

735  

736 global __cuCtxGetStreamPriorityRange 

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

738  

739 global __cuCtxResetPersistingL2Cache 

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

741  

742 global __cuCtxGetExecAffinity 

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

744  

745 global __cuCtxRecordEvent 

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

747  

748 global __cuCtxWaitEvent 

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

750  

751 global __cuCtxAttach 

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

753  

754 global __cuCtxDetach 

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

756  

757 global __cuCtxGetSharedMemConfig 

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

759  

760 global __cuCtxSetSharedMemConfig 

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

762  

763 global __cuModuleLoad 

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

765  

766 global __cuModuleLoadData 

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

768  

769 global __cuModuleLoadDataEx 

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

771  

772 global __cuModuleLoadFatBinary 

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

774  

775 global __cuModuleUnload 

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

777  

778 global __cuModuleGetLoadingMode 

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

780  

781 global __cuModuleGetFunction 

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

783  

784 global __cuModuleGetFunctionCount 

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

786  

787 global __cuModuleEnumerateFunctions 

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

789  

790 global __cuModuleGetGlobal_v2 

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

792  

793 global __cuLinkCreate_v2 

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

795  

796 global __cuLinkAddData_v2 

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

798  

799 global __cuLinkAddFile_v2 

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

801  

802 global __cuLinkComplete 

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

804  

805 global __cuLinkDestroy 

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

807  

808 global __cuModuleGetTexRef 

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

810  

811 global __cuModuleGetSurfRef 

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

813  

814 global __cuLibraryLoadData 

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

816  

817 global __cuLibraryLoadFromFile 

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

819  

820 global __cuLibraryUnload 

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

822  

823 global __cuLibraryGetKernel 

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

825  

826 global __cuLibraryGetKernelCount 

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

828  

829 global __cuLibraryEnumerateKernels 

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

831  

832 global __cuLibraryGetModule 

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

834  

835 global __cuKernelGetFunction 

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

837  

838 global __cuKernelGetLibrary 

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

840  

841 global __cuLibraryGetGlobal 

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

843  

844 global __cuLibraryGetManaged 

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

846  

847 global __cuLibraryGetUnifiedFunction 

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

849  

850 global __cuKernelGetAttribute 

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

852  

853 global __cuKernelSetAttribute 

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

855  

856 global __cuKernelSetCacheConfig 

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

858  

859 global __cuKernelGetName 

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

861  

862 global __cuKernelGetParamInfo 

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

864  

865 global __cuMemGetInfo_v2 

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

867  

868 global __cuMemAlloc_v2 

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

870  

871 global __cuMemAllocPitch_v2 

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

873  

874 global __cuMemFree_v2 

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

876  

877 global __cuMemGetAddressRange_v2 

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

879  

880 global __cuMemAllocHost_v2 

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

882  

883 global __cuMemFreeHost 

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

885  

886 global __cuMemHostAlloc 

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

888  

889 global __cuMemHostGetDevicePointer_v2 

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

891  

892 global __cuMemHostGetFlags 

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

894  

895 global __cuMemAllocManaged 

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

897  

898 global __cuDeviceRegisterAsyncNotification 

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

900  

901 global __cuDeviceUnregisterAsyncNotification 

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

903  

904 global __cuDeviceGetByPCIBusId 

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

906  

907 global __cuDeviceGetPCIBusId 

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

909  

910 global __cuIpcGetEventHandle 

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

912  

913 global __cuIpcOpenEventHandle 

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

915  

916 global __cuIpcGetMemHandle 

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

918  

919 global __cuIpcOpenMemHandle_v2 

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

921  

922 global __cuIpcCloseMemHandle 

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

924  

925 global __cuMemHostRegister_v2 

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

927  

928 global __cuMemHostUnregister 

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

930  

931 global __cuMemcpy 

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

933  

934 global __cuMemcpyPeer 

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

936  

937 global __cuMemcpyHtoD_v2 

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

939  

940 global __cuMemcpyDtoH_v2 

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

942  

943 global __cuMemcpyDtoD_v2 

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

945  

946 global __cuMemcpyDtoA_v2 

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

948  

949 global __cuMemcpyAtoD_v2 

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

951  

952 global __cuMemcpyHtoA_v2 

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

954  

955 global __cuMemcpyAtoH_v2 

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

957  

958 global __cuMemcpyAtoA_v2 

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

960  

961 global __cuMemcpy2D_v2 

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

963  

964 global __cuMemcpy2DUnaligned_v2 

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

966  

967 global __cuMemcpy3D_v2 

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

969  

970 global __cuMemcpy3DPeer 

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

972  

973 global __cuMemcpyAsync 

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

975  

976 global __cuMemcpyPeerAsync 

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

978  

979 global __cuMemcpyHtoDAsync_v2 

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

981  

982 global __cuMemcpyDtoHAsync_v2 

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

984  

985 global __cuMemcpyDtoDAsync_v2 

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

987  

988 global __cuMemcpyHtoAAsync_v2 

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

990  

991 global __cuMemcpyAtoHAsync_v2 

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

993  

994 global __cuMemcpy2DAsync_v2 

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

996  

997 global __cuMemcpy3DAsync_v2 

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

999  

1000 global __cuMemcpy3DPeerAsync 

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

1002  

1003 global __cuMemsetD8_v2 

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

1005  

1006 global __cuMemsetD16_v2 

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

1008  

1009 global __cuMemsetD32_v2 

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

1011  

1012 global __cuMemsetD2D8_v2 

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

1014  

1015 global __cuMemsetD2D16_v2 

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

1017  

1018 global __cuMemsetD2D32_v2 

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

1020  

1021 global __cuMemsetD8Async 

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

1023  

1024 global __cuMemsetD16Async 

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

1026  

1027 global __cuMemsetD32Async 

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

1029  

1030 global __cuMemsetD2D8Async 

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

1032  

1033 global __cuMemsetD2D16Async 

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

1035  

1036 global __cuMemsetD2D32Async 

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

1038  

1039 global __cuArrayCreate_v2 

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

1041  

1042 global __cuArrayGetDescriptor_v2 

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

1044  

1045 global __cuArrayGetSparseProperties 

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

1047  

1048 global __cuMipmappedArrayGetSparseProperties 

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

1050  

1051 global __cuArrayGetMemoryRequirements 

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

1053  

1054 global __cuMipmappedArrayGetMemoryRequirements 

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

1056  

1057 global __cuArrayGetPlane 

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

1059  

1060 global __cuArrayDestroy 

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

1062  

1063 global __cuArray3DCreate_v2 

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

1065  

1066 global __cuArray3DGetDescriptor_v2 

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

1068  

1069 global __cuMipmappedArrayCreate 

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

1071  

1072 global __cuMipmappedArrayGetLevel 

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

1074  

1075 global __cuMipmappedArrayDestroy 

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

1077  

1078 global __cuMemGetHandleForAddressRange 

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

1080  

1081 global __cuMemBatchDecompressAsync 

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

1083  

1084 global __cuMemAddressReserve 

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

1086  

1087 global __cuMemAddressFree 

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

1089  

1090 global __cuMemCreate 

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

1092  

1093 global __cuMemRelease 

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

1095  

1096 global __cuMemMap 

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

1098  

1099 global __cuMemMapArrayAsync 

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

1101  

1102 global __cuMemUnmap 

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

1104  

1105 global __cuMemSetAccess 

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

1107  

1108 global __cuMemGetAccess 

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

1110  

1111 global __cuMemExportToShareableHandle 

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

1113  

1114 global __cuMemImportFromShareableHandle 

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

1116  

1117 global __cuMemGetAllocationGranularity 

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

1119  

1120 global __cuMemGetAllocationPropertiesFromHandle 

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

1122  

1123 global __cuMemRetainAllocationHandle 

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

1125  

1126 global __cuMemFreeAsync 

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

1128  

1129 global __cuMemAllocAsync 

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

1131  

1132 global __cuMemPoolTrimTo 

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

1134  

1135 global __cuMemPoolSetAttribute 

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

1137  

1138 global __cuMemPoolGetAttribute 

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

1140  

1141 global __cuMemPoolSetAccess 

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

1143  

1144 global __cuMemPoolGetAccess 

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

1146  

1147 global __cuMemPoolCreate 

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

1149  

1150 global __cuMemPoolDestroy 

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

1152  

1153 global __cuMemAllocFromPoolAsync 

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

1155  

1156 global __cuMemPoolExportToShareableHandle 

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

1158  

1159 global __cuMemPoolImportFromShareableHandle 

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

1161  

1162 global __cuMemPoolExportPointer 

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

1164  

1165 global __cuMemPoolImportPointer 

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

1167  

1168 global __cuMulticastCreate 

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

1170  

1171 global __cuMulticastAddDevice 

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

1173  

1174 global __cuMulticastBindMem 

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

1176  

1177 global __cuMulticastBindAddr 

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

1179  

1180 global __cuMulticastUnbind 

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

1182  

1183 global __cuMulticastGetGranularity 

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

1185  

1186 global __cuPointerGetAttribute 

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

1188  

1189 global __cuMemPrefetchAsync_v2 

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

1191  

1192 global __cuMemAdvise_v2 

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

1194  

1195 global __cuMemRangeGetAttribute 

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

1197  

1198 global __cuMemRangeGetAttributes 

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

1200  

1201 global __cuPointerSetAttribute 

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

1203  

1204 global __cuPointerGetAttributes 

1205 cuGetProcAddress_v2('cuPointerGetAttributes', <void **>&__cuPointerGetAttributes, 7000, ptds_mode, NULL) (empty)

1206  

1207 global __cuStreamCreate 

1208 cuGetProcAddress_v2('cuStreamCreate', <void **>&__cuStreamCreate, 2000, ptds_mode, NULL) (empty)

1209  

1210 global __cuStreamCreateWithPriority 

1211 cuGetProcAddress_v2('cuStreamCreateWithPriority', <void **>&__cuStreamCreateWithPriority, 5050, ptds_mode, NULL) (empty)