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

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

2# 

3# SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE 

4# 

5# This code was automatically generated across versions from 12.9.0 to 13.3.0, generator version 0.3.1.dev1738+g1060a290f. Do not modify it directly. 

6  

7from libc.stdint cimport intptr_t, uintptr_t 

8  

9import os (empty)

10import threading (empty)

11from .utils import FunctionNotFoundError, NotSupportedError (empty)

12  

13from cuda.pathfinder import load_nvidia_dynamic_lib (empty)

14  

15  

16############################################################################### 

17# Extern 

18############################################################################### 

19  

20# You must 'from .utils import NotSupportedError' before using this template 

21  

22cdef extern from "<dlfcn.h>" nogil: 

23 void* dlopen(const char*, int) 

24 char* dlerror() 

25 void* dlsym(void*, const char*) 

26 int dlclose(void*) 

27  

28 enum: 

29 RTLD_LAZY 

30 RTLD_NOW 

31 RTLD_GLOBAL 

32 RTLD_LOCAL 

33  

34 const void* RTLD_DEFAULT 'RTLD_DEFAULT' 

35  

36cdef int get_cuda_version(): (empty)

37 cdef void* handle = NULL 

38 cdef int err, driver_ver = 0 

39  

40 # Load driver to check version 

41 handle = dlopen('libcuda.so.1', RTLD_NOW | RTLD_GLOBAL) (empty)

42 if handle == NULL: 

43 err_msg = dlerror() 

44 raise NotSupportedError(f'CUDA driver is not found ({err_msg.decode()})') 

45 cuDriverGetVersion = dlsym(handle, "cuDriverGetVersion") 

46 if cuDriverGetVersion == NULL: 

47 raise RuntimeError('Did not find cuDriverGetVersion symbol in libcuda.so.1') 

48 err = (<int (*)(int*) noexcept nogil>cuDriverGetVersion)(&driver_ver) 

49 if err != 0: 

50 raise RuntimeError(f'cuDriverGetVersion returned error code {err}') 

51  

52 return driver_ver 

53  

54  

55  

56############################################################################### 

57# Wrapper init 

58############################################################################### 

59  

60cdef object __symbol_lock = threading.Lock() (empty)

61cdef bint __py_driver_init = False (empty)

62  

63cdef void* __cuGetErrorString = NULL (empty)

64cdef void* __cuGetErrorName = NULL (empty)

65cdef void* __cuInit = NULL (empty)

66cdef void* __cuDriverGetVersion = NULL (empty)

67cdef void* __cuDeviceGet = NULL (empty)

68cdef void* __cuDeviceGetCount = NULL (empty)

69cdef void* __cuDeviceGetName = NULL (empty)

70cdef void* __cuDeviceGetUuid_v2 = NULL (empty)

71cdef void* __cuDeviceGetLuid = NULL (empty)

72cdef void* __cuDeviceTotalMem_v2 = NULL (empty)

73cdef void* __cuDeviceGetTexture1DLinearMaxWidth = NULL (empty)

74cdef void* __cuDeviceGetAttribute = NULL (empty)

75cdef void* __cuDeviceGetNvSciSyncAttributes = NULL (empty)

76cdef void* __cuDeviceSetMemPool = NULL (empty)

77cdef void* __cuDeviceGetMemPool = NULL (empty)

78cdef void* __cuDeviceGetDefaultMemPool = NULL (empty)

79cdef void* __cuDeviceGetExecAffinitySupport = NULL (empty)

80cdef void* __cuFlushGPUDirectRDMAWrites = NULL (empty)

81cdef void* __cuDeviceGetProperties = NULL (empty)

82cdef void* __cuDeviceComputeCapability = NULL (empty)

83cdef void* __cuDevicePrimaryCtxRetain = NULL (empty)

84cdef void* __cuDevicePrimaryCtxRelease_v2 = NULL (empty)

85cdef void* __cuDevicePrimaryCtxSetFlags_v2 = NULL (empty)

86cdef void* __cuDevicePrimaryCtxGetState = NULL (empty)

87cdef void* __cuDevicePrimaryCtxReset_v2 = NULL (empty)

88cdef void* __cuCtxCreate_v4 = NULL (empty)

89cdef void* __cuCtxDestroy_v2 = NULL (empty)

90cdef void* __cuCtxPushCurrent_v2 = NULL (empty)

91cdef void* __cuCtxPopCurrent_v2 = NULL (empty)

92cdef void* __cuCtxSetCurrent = NULL (empty)

93cdef void* __cuCtxGetCurrent = NULL (empty)

94cdef void* __cuCtxGetDevice = NULL (empty)

95cdef void* __cuCtxGetFlags = NULL (empty)

96cdef void* __cuCtxSetFlags = NULL (empty)

97cdef void* __cuCtxGetId = NULL (empty)

98cdef void* __cuCtxSynchronize = NULL (empty)

99cdef void* __cuCtxSetLimit = NULL (empty)

100cdef void* __cuCtxGetLimit = NULL (empty)

101cdef void* __cuCtxGetCacheConfig = NULL (empty)

102cdef void* __cuCtxSetCacheConfig = NULL (empty)

103cdef void* __cuCtxGetApiVersion = NULL (empty)

104cdef void* __cuCtxGetStreamPriorityRange = NULL (empty)

105cdef void* __cuCtxResetPersistingL2Cache = NULL (empty)

106cdef void* __cuCtxGetExecAffinity = NULL (empty)

107cdef void* __cuCtxRecordEvent = NULL (empty)

108cdef void* __cuCtxWaitEvent = NULL (empty)

109cdef void* __cuCtxAttach = NULL (empty)

110cdef void* __cuCtxDetach = NULL (empty)

111cdef void* __cuCtxGetSharedMemConfig = NULL (empty)

112cdef void* __cuCtxSetSharedMemConfig = NULL (empty)

113cdef void* __cuModuleLoad = NULL (empty)

114cdef void* __cuModuleLoadData = NULL (empty)

115cdef void* __cuModuleLoadDataEx = NULL (empty)

116cdef void* __cuModuleLoadFatBinary = NULL (empty)

117cdef void* __cuModuleUnload = NULL (empty)

118cdef void* __cuModuleGetLoadingMode = NULL (empty)

119cdef void* __cuModuleGetFunction = NULL (empty)

120cdef void* __cuModuleGetFunctionCount = NULL (empty)

121cdef void* __cuModuleEnumerateFunctions = NULL (empty)

122cdef void* __cuModuleGetGlobal_v2 = NULL (empty)

123cdef void* __cuLinkCreate_v2 = NULL (empty)

124cdef void* __cuLinkAddData_v2 = NULL (empty)

125cdef void* __cuLinkAddFile_v2 = NULL (empty)

126cdef void* __cuLinkComplete = NULL (empty)

127cdef void* __cuLinkDestroy = NULL (empty)

128cdef void* __cuModuleGetTexRef = NULL (empty)

129cdef void* __cuModuleGetSurfRef = NULL (empty)

130cdef void* __cuLibraryLoadData = NULL (empty)

131cdef void* __cuLibraryLoadFromFile = NULL (empty)

132cdef void* __cuLibraryUnload = NULL (empty)

133cdef void* __cuLibraryGetKernel = NULL (empty)

134cdef void* __cuLibraryGetKernelCount = NULL (empty)

135cdef void* __cuLibraryEnumerateKernels = NULL (empty)

136cdef void* __cuLibraryGetModule = NULL (empty)

137cdef void* __cuKernelGetFunction = NULL (empty)

138cdef void* __cuKernelGetLibrary = NULL (empty)

139cdef void* __cuLibraryGetGlobal = NULL (empty)

140cdef void* __cuLibraryGetManaged = NULL (empty)

141cdef void* __cuLibraryGetUnifiedFunction = NULL (empty)

142cdef void* __cuKernelGetAttribute = NULL (empty)

143cdef void* __cuKernelSetAttribute = NULL (empty)

144cdef void* __cuKernelSetCacheConfig = NULL (empty)

145cdef void* __cuKernelGetName = NULL (empty)

146cdef void* __cuKernelGetParamInfo = NULL (empty)

147cdef void* __cuMemGetInfo_v2 = NULL (empty)

148cdef void* __cuMemAlloc_v2 = NULL (empty)

149cdef void* __cuMemAllocPitch_v2 = NULL (empty)

150cdef void* __cuMemFree_v2 = NULL (empty)

151cdef void* __cuMemGetAddressRange_v2 = NULL (empty)

152cdef void* __cuMemAllocHost_v2 = NULL (empty)

153cdef void* __cuMemFreeHost = NULL (empty)

154cdef void* __cuMemHostAlloc = NULL (empty)

155cdef void* __cuMemHostGetDevicePointer_v2 = NULL (empty)

156cdef void* __cuMemHostGetFlags = NULL (empty)

157cdef void* __cuMemAllocManaged = NULL (empty)

158cdef void* __cuDeviceRegisterAsyncNotification = NULL (empty)

159cdef void* __cuDeviceUnregisterAsyncNotification = NULL (empty)

160cdef void* __cuDeviceGetByPCIBusId = NULL (empty)

161cdef void* __cuDeviceGetPCIBusId = NULL (empty)

162cdef void* __cuIpcGetEventHandle = NULL (empty)

163cdef void* __cuIpcOpenEventHandle = NULL (empty)

164cdef void* __cuIpcGetMemHandle = NULL (empty)

165cdef void* __cuIpcOpenMemHandle_v2 = NULL (empty)

166cdef void* __cuIpcCloseMemHandle = NULL (empty)

167cdef void* __cuMemHostRegister_v2 = NULL (empty)

168cdef void* __cuMemHostUnregister = NULL (empty)

169cdef void* __cuMemcpy = NULL (empty)

170cdef void* __cuMemcpyPeer = NULL (empty)

171cdef void* __cuMemcpyHtoD_v2 = NULL (empty)

172cdef void* __cuMemcpyDtoH_v2 = NULL (empty)

173cdef void* __cuMemcpyDtoD_v2 = NULL (empty)

174cdef void* __cuMemcpyDtoA_v2 = NULL (empty)

175cdef void* __cuMemcpyAtoD_v2 = NULL (empty)

176cdef void* __cuMemcpyHtoA_v2 = NULL (empty)

177cdef void* __cuMemcpyAtoH_v2 = NULL (empty)

178cdef void* __cuMemcpyAtoA_v2 = NULL (empty)

179cdef void* __cuMemcpy2D_v2 = NULL (empty)

180cdef void* __cuMemcpy2DUnaligned_v2 = NULL (empty)

181cdef void* __cuMemcpy3D_v2 = NULL (empty)

182cdef void* __cuMemcpy3DPeer = NULL (empty)

183cdef void* __cuMemcpyAsync = NULL (empty)

184cdef void* __cuMemcpyPeerAsync = NULL (empty)

185cdef void* __cuMemcpyHtoDAsync_v2 = NULL (empty)

186cdef void* __cuMemcpyDtoHAsync_v2 = NULL (empty)

187cdef void* __cuMemcpyDtoDAsync_v2 = NULL (empty)

188cdef void* __cuMemcpyHtoAAsync_v2 = NULL (empty)

189cdef void* __cuMemcpyAtoHAsync_v2 = NULL (empty)

190cdef void* __cuMemcpy2DAsync_v2 = NULL (empty)

191cdef void* __cuMemcpy3DAsync_v2 = NULL (empty)

192cdef void* __cuMemcpy3DPeerAsync = NULL (empty)

193cdef void* __cuMemsetD8_v2 = NULL (empty)

194cdef void* __cuMemsetD16_v2 = NULL (empty)

195cdef void* __cuMemsetD32_v2 = NULL (empty)

196cdef void* __cuMemsetD2D8_v2 = NULL (empty)

197cdef void* __cuMemsetD2D16_v2 = NULL (empty)

198cdef void* __cuMemsetD2D32_v2 = NULL (empty)

199cdef void* __cuMemsetD8Async = NULL (empty)

200cdef void* __cuMemsetD16Async = NULL (empty)

201cdef void* __cuMemsetD32Async = NULL (empty)

202cdef void* __cuMemsetD2D8Async = NULL (empty)

203cdef void* __cuMemsetD2D16Async = NULL (empty)

204cdef void* __cuMemsetD2D32Async = NULL (empty)

205cdef void* __cuArrayCreate_v2 = NULL (empty)

206cdef void* __cuArrayGetDescriptor_v2 = NULL (empty)

207cdef void* __cuArrayGetSparseProperties = NULL (empty)

208cdef void* __cuMipmappedArrayGetSparseProperties = NULL (empty)

209cdef void* __cuArrayGetMemoryRequirements = NULL (empty)

210cdef void* __cuMipmappedArrayGetMemoryRequirements = NULL (empty)

211cdef void* __cuArrayGetPlane = NULL (empty)

212cdef void* __cuArrayDestroy = NULL (empty)

213cdef void* __cuArray3DCreate_v2 = NULL (empty)

214cdef void* __cuArray3DGetDescriptor_v2 = NULL (empty)

215cdef void* __cuMipmappedArrayCreate = NULL (empty)

216cdef void* __cuMipmappedArrayGetLevel = NULL (empty)

217cdef void* __cuMipmappedArrayDestroy = NULL (empty)

218cdef void* __cuMemGetHandleForAddressRange = NULL (empty)

219cdef void* __cuMemBatchDecompressAsync = NULL (empty)

220cdef void* __cuMemAddressReserve = NULL (empty)

221cdef void* __cuMemAddressFree = NULL (empty)

222cdef void* __cuMemCreate = NULL (empty)

223cdef void* __cuMemRelease = NULL (empty)

224cdef void* __cuMemMap = NULL (empty)

225cdef void* __cuMemMapArrayAsync = NULL (empty)

226cdef void* __cuMemUnmap = NULL (empty)

227cdef void* __cuMemSetAccess = NULL (empty)

228cdef void* __cuMemGetAccess = NULL (empty)

229cdef void* __cuMemExportToShareableHandle = NULL (empty)

230cdef void* __cuMemImportFromShareableHandle = NULL (empty)

231cdef void* __cuMemGetAllocationGranularity = NULL (empty)

232cdef void* __cuMemGetAllocationPropertiesFromHandle = NULL (empty)

233cdef void* __cuMemRetainAllocationHandle = NULL (empty)

234cdef void* __cuMemFreeAsync = NULL (empty)

235cdef void* __cuMemAllocAsync = NULL (empty)

236cdef void* __cuMemPoolTrimTo = NULL (empty)

237cdef void* __cuMemPoolSetAttribute = NULL (empty)

238cdef void* __cuMemPoolGetAttribute = NULL (empty)

239cdef void* __cuMemPoolSetAccess = NULL (empty)

240cdef void* __cuMemPoolGetAccess = NULL (empty)

241cdef void* __cuMemPoolCreate = NULL (empty)

242cdef void* __cuMemPoolDestroy = NULL (empty)

243cdef void* __cuMemAllocFromPoolAsync = NULL (empty)

244cdef void* __cuMemPoolExportToShareableHandle = NULL (empty)

245cdef void* __cuMemPoolImportFromShareableHandle = NULL (empty)

246cdef void* __cuMemPoolExportPointer = NULL (empty)

247cdef void* __cuMemPoolImportPointer = NULL (empty)

248cdef void* __cuMulticastCreate = NULL (empty)

249cdef void* __cuMulticastAddDevice = NULL (empty)

250cdef void* __cuMulticastBindMem = NULL (empty)

251cdef void* __cuMulticastBindAddr = NULL (empty)

252cdef void* __cuMulticastUnbind = NULL (empty)

253cdef void* __cuMulticastGetGranularity = NULL (empty)

254cdef void* __cuPointerGetAttribute = NULL (empty)

255cdef void* __cuMemPrefetchAsync_v2 = NULL (empty)

256cdef void* __cuMemAdvise_v2 = NULL (empty)

257cdef void* __cuMemRangeGetAttribute = NULL (empty)

258cdef void* __cuMemRangeGetAttributes = NULL (empty)

259cdef void* __cuPointerSetAttribute = NULL (empty)

260cdef void* __cuPointerGetAttributes = NULL (empty)

261cdef void* __cuStreamCreate = NULL (empty)

262cdef void* __cuStreamCreateWithPriority = NULL (empty)

263cdef void* __cuStreamGetPriority = NULL (empty)

264cdef void* __cuStreamGetDevice = NULL (empty)

265cdef void* __cuStreamGetFlags = NULL (empty)

266cdef void* __cuStreamGetId = NULL (empty)

267cdef void* __cuStreamGetCtx = NULL (empty)

268cdef void* __cuStreamGetCtx_v2 = NULL (empty)

269cdef void* __cuStreamWaitEvent = NULL (empty)

270cdef void* __cuStreamAddCallback = NULL (empty)

271cdef void* __cuStreamBeginCapture_v2 = NULL (empty)

272cdef void* __cuStreamBeginCaptureToGraph = NULL (empty)

273cdef void* __cuThreadExchangeStreamCaptureMode = NULL (empty)

274cdef void* __cuStreamEndCapture = NULL (empty)

275cdef void* __cuStreamIsCapturing = NULL (empty)

276cdef void* __cuStreamGetCaptureInfo_v3 = NULL (empty)

277cdef void* __cuStreamUpdateCaptureDependencies_v2 = NULL (empty)

278cdef void* __cuStreamAttachMemAsync = NULL (empty)

279cdef void* __cuStreamQuery = NULL (empty)

280cdef void* __cuStreamSynchronize = NULL (empty)

281cdef void* __cuStreamDestroy_v2 = NULL (empty)

282cdef void* __cuStreamCopyAttributes = NULL (empty)

283cdef void* __cuStreamGetAttribute = NULL (empty)

284cdef void* __cuStreamSetAttribute = NULL (empty)

285cdef void* __cuEventCreate = NULL (empty)

286cdef void* __cuEventRecord = NULL (empty)

287cdef void* __cuEventRecordWithFlags = NULL (empty)

288cdef void* __cuEventQuery = NULL (empty)

289cdef void* __cuEventSynchronize = NULL (empty)

290cdef void* __cuEventDestroy_v2 = NULL (empty)

291cdef void* __cuEventElapsedTime_v2 = NULL (empty)

292cdef void* __cuImportExternalMemory = NULL (empty)

293cdef void* __cuExternalMemoryGetMappedBuffer = NULL (empty)

294cdef void* __cuExternalMemoryGetMappedMipmappedArray = NULL (empty)

295cdef void* __cuDestroyExternalMemory = NULL (empty)

296cdef void* __cuImportExternalSemaphore = NULL (empty)

297cdef void* __cuSignalExternalSemaphoresAsync = NULL (empty)

298cdef void* __cuWaitExternalSemaphoresAsync = NULL (empty)

299cdef void* __cuDestroyExternalSemaphore = NULL (empty)

300cdef void* __cuStreamWaitValue32_v2 = NULL (empty)

301cdef void* __cuStreamWaitValue64_v2 = NULL (empty)

302cdef void* __cuStreamWriteValue32_v2 = NULL (empty)

303cdef void* __cuStreamWriteValue64_v2 = NULL (empty)

304cdef void* __cuStreamBatchMemOp_v2 = NULL (empty)

305cdef void* __cuFuncGetAttribute = NULL (empty)

306cdef void* __cuFuncSetAttribute = NULL (empty)

307cdef void* __cuFuncSetCacheConfig = NULL (empty)

308cdef void* __cuFuncGetModule = NULL (empty)

309cdef void* __cuFuncGetName = NULL (empty)

310cdef void* __cuFuncGetParamInfo = NULL (empty)

311cdef void* __cuFuncIsLoaded = NULL (empty)

312cdef void* __cuFuncLoad = NULL (empty)

313cdef void* __cuLaunchKernel = NULL (empty)

314cdef void* __cuLaunchKernelEx = NULL (empty)

315cdef void* __cuLaunchCooperativeKernel = NULL (empty)

316cdef void* __cuLaunchCooperativeKernelMultiDevice = NULL (empty)

317cdef void* __cuLaunchHostFunc = NULL (empty)

318cdef void* __cuFuncSetBlockShape = NULL (empty)

319cdef void* __cuFuncSetSharedSize = NULL (empty)

320cdef void* __cuParamSetSize = NULL (empty)

321cdef void* __cuParamSeti = NULL (empty)

322cdef void* __cuParamSetf = NULL (empty)

323cdef void* __cuParamSetv = NULL (empty)

324cdef void* __cuLaunch = NULL (empty)

325cdef void* __cuLaunchGrid = NULL (empty)

326cdef void* __cuLaunchGridAsync = NULL (empty)

327cdef void* __cuParamSetTexRef = NULL (empty)

328cdef void* __cuFuncSetSharedMemConfig = NULL (empty)

329cdef void* __cuGraphCreate = NULL (empty)

330cdef void* __cuGraphAddKernelNode_v2 = NULL (empty)

331cdef void* __cuGraphKernelNodeGetParams_v2 = NULL (empty)

332cdef void* __cuGraphKernelNodeSetParams_v2 = NULL (empty)

333cdef void* __cuGraphAddMemcpyNode = NULL (empty)

334cdef void* __cuGraphMemcpyNodeGetParams = NULL (empty)

335cdef void* __cuGraphMemcpyNodeSetParams = NULL (empty)

336cdef void* __cuGraphAddMemsetNode = NULL (empty)

337cdef void* __cuGraphMemsetNodeGetParams = NULL (empty)

338cdef void* __cuGraphMemsetNodeSetParams = NULL (empty)

339cdef void* __cuGraphAddHostNode = NULL (empty)

340cdef void* __cuGraphHostNodeGetParams = NULL (empty)

341cdef void* __cuGraphHostNodeSetParams = NULL (empty)

342cdef void* __cuGraphAddChildGraphNode = NULL (empty)

343cdef void* __cuGraphChildGraphNodeGetGraph = NULL (empty)

344cdef void* __cuGraphAddEmptyNode = NULL (empty)

345cdef void* __cuGraphAddEventRecordNode = NULL (empty)

346cdef void* __cuGraphEventRecordNodeGetEvent = NULL (empty)

347cdef void* __cuGraphEventRecordNodeSetEvent = NULL (empty)

348cdef void* __cuGraphAddEventWaitNode = NULL (empty)

349cdef void* __cuGraphEventWaitNodeGetEvent = NULL (empty)

350cdef void* __cuGraphEventWaitNodeSetEvent = NULL (empty)

351cdef void* __cuGraphAddExternalSemaphoresSignalNode = NULL (empty)

352cdef void* __cuGraphExternalSemaphoresSignalNodeGetParams = NULL (empty)

353cdef void* __cuGraphExternalSemaphoresSignalNodeSetParams = NULL (empty)

354cdef void* __cuGraphAddExternalSemaphoresWaitNode = NULL (empty)

355cdef void* __cuGraphExternalSemaphoresWaitNodeGetParams = NULL (empty)

356cdef void* __cuGraphExternalSemaphoresWaitNodeSetParams = NULL (empty)

357cdef void* __cuGraphAddBatchMemOpNode = NULL (empty)

358cdef void* __cuGraphBatchMemOpNodeGetParams = NULL (empty)

359cdef void* __cuGraphBatchMemOpNodeSetParams = NULL (empty)

360cdef void* __cuGraphExecBatchMemOpNodeSetParams = NULL (empty)

361cdef void* __cuGraphAddMemAllocNode = NULL (empty)

362cdef void* __cuGraphMemAllocNodeGetParams = NULL (empty)

363cdef void* __cuGraphAddMemFreeNode = NULL (empty)

364cdef void* __cuGraphMemFreeNodeGetParams = NULL (empty)

365cdef void* __cuDeviceGraphMemTrim = NULL (empty)

366cdef void* __cuDeviceGetGraphMemAttribute = NULL (empty)

367cdef void* __cuDeviceSetGraphMemAttribute = NULL (empty)

368cdef void* __cuGraphClone = NULL (empty)

369cdef void* __cuGraphNodeFindInClone = NULL (empty)

370cdef void* __cuGraphNodeGetType = NULL (empty)

371cdef void* __cuGraphGetNodes = NULL (empty)

372cdef void* __cuGraphGetRootNodes = NULL (empty)

373cdef void* __cuGraphGetEdges_v2 = NULL (empty)

374cdef void* __cuGraphNodeGetDependencies_v2 = NULL (empty)

375cdef void* __cuGraphNodeGetDependentNodes_v2 = NULL (empty)

376cdef void* __cuGraphAddDependencies_v2 = NULL (empty)

377cdef void* __cuGraphRemoveDependencies_v2 = NULL (empty)

378cdef void* __cuGraphDestroyNode = NULL (empty)

379cdef void* __cuGraphInstantiateWithFlags = NULL (empty)

380cdef void* __cuGraphInstantiateWithParams = NULL (empty)

381cdef void* __cuGraphExecGetFlags = NULL (empty)

382cdef void* __cuGraphExecKernelNodeSetParams_v2 = NULL (empty)

383cdef void* __cuGraphExecMemcpyNodeSetParams = NULL (empty)

384cdef void* __cuGraphExecMemsetNodeSetParams = NULL (empty)

385cdef void* __cuGraphExecHostNodeSetParams = NULL (empty)

386cdef void* __cuGraphExecChildGraphNodeSetParams = NULL (empty)

387cdef void* __cuGraphExecEventRecordNodeSetEvent = NULL (empty)

388cdef void* __cuGraphExecEventWaitNodeSetEvent = NULL (empty)

389cdef void* __cuGraphExecExternalSemaphoresSignalNodeSetParams = NULL (empty)

390cdef void* __cuGraphExecExternalSemaphoresWaitNodeSetParams = NULL (empty)

391cdef void* __cuGraphNodeSetEnabled = NULL (empty)

392cdef void* __cuGraphNodeGetEnabled = NULL (empty)

393cdef void* __cuGraphUpload = NULL (empty)

394cdef void* __cuGraphLaunch = NULL (empty)

395cdef void* __cuGraphExecDestroy = NULL (empty)

396cdef void* __cuGraphDestroy = NULL (empty)

397cdef void* __cuGraphExecUpdate_v2 = NULL (empty)

398cdef void* __cuGraphKernelNodeCopyAttributes = NULL (empty)

399cdef void* __cuGraphKernelNodeGetAttribute = NULL (empty)

400cdef void* __cuGraphKernelNodeSetAttribute = NULL (empty)

401cdef void* __cuGraphDebugDotPrint = NULL (empty)

402cdef void* __cuUserObjectCreate = NULL (empty)

403cdef void* __cuUserObjectRetain = NULL (empty)

404cdef void* __cuUserObjectRelease = NULL (empty)

405cdef void* __cuGraphRetainUserObject = NULL (empty)

406cdef void* __cuGraphReleaseUserObject = NULL (empty)

407cdef void* __cuGraphAddNode_v2 = NULL (empty)

408cdef void* __cuGraphNodeSetParams = NULL (empty)

409cdef void* __cuGraphExecNodeSetParams = NULL (empty)

410cdef void* __cuGraphConditionalHandleCreate = NULL (empty)

411cdef void* __cuOccupancyMaxActiveBlocksPerMultiprocessor = NULL (empty)

412cdef void* __cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags = NULL (empty)

413cdef void* __cuOccupancyMaxPotentialBlockSize = NULL (empty)

414cdef void* __cuOccupancyMaxPotentialBlockSizeWithFlags = NULL (empty)

415cdef void* __cuOccupancyAvailableDynamicSMemPerBlock = NULL (empty)

416cdef void* __cuOccupancyMaxPotentialClusterSize = NULL (empty)

417cdef void* __cuOccupancyMaxActiveClusters = NULL (empty)

418cdef void* __cuTexRefSetArray = NULL (empty)

419cdef void* __cuTexRefSetMipmappedArray = NULL (empty)

420cdef void* __cuTexRefSetAddress_v2 = NULL (empty)

421cdef void* __cuTexRefSetAddress2D_v3 = NULL (empty)

422cdef void* __cuTexRefSetFormat = NULL (empty)

423cdef void* __cuTexRefSetAddressMode = NULL (empty)

424cdef void* __cuTexRefSetFilterMode = NULL (empty)

425cdef void* __cuTexRefSetMipmapFilterMode = NULL (empty)

426cdef void* __cuTexRefSetMipmapLevelBias = NULL (empty)

427cdef void* __cuTexRefSetMipmapLevelClamp = NULL (empty)

428cdef void* __cuTexRefSetMaxAnisotropy = NULL (empty)

429cdef void* __cuTexRefSetBorderColor = NULL (empty)

430cdef void* __cuTexRefSetFlags = NULL (empty)

431cdef void* __cuTexRefGetAddress_v2 = NULL (empty)

432cdef void* __cuTexRefGetArray = NULL (empty)

433cdef void* __cuTexRefGetMipmappedArray = NULL (empty)

434cdef void* __cuTexRefGetAddressMode = NULL (empty)

435cdef void* __cuTexRefGetFilterMode = NULL (empty)

436cdef void* __cuTexRefGetFormat = NULL (empty)

437cdef void* __cuTexRefGetMipmapFilterMode = NULL (empty)

438cdef void* __cuTexRefGetMipmapLevelBias = NULL (empty)

439cdef void* __cuTexRefGetMipmapLevelClamp = NULL (empty)

440cdef void* __cuTexRefGetMaxAnisotropy = NULL (empty)

441cdef void* __cuTexRefGetBorderColor = NULL (empty)

442cdef void* __cuTexRefGetFlags = NULL (empty)

443cdef void* __cuTexRefCreate = NULL (empty)

444cdef void* __cuTexRefDestroy = NULL (empty)

445cdef void* __cuSurfRefSetArray = NULL (empty)

446cdef void* __cuSurfRefGetArray = NULL (empty)

447cdef void* __cuTexObjectCreate = NULL (empty)

448cdef void* __cuTexObjectDestroy = NULL (empty)

449cdef void* __cuTexObjectGetResourceDesc = NULL (empty)

450cdef void* __cuTexObjectGetTextureDesc = NULL (empty)

451cdef void* __cuTexObjectGetResourceViewDesc = NULL (empty)

452cdef void* __cuSurfObjectCreate = NULL (empty)

453cdef void* __cuSurfObjectDestroy = NULL (empty)

454cdef void* __cuSurfObjectGetResourceDesc = NULL (empty)

455cdef void* __cuTensorMapEncodeTiled = NULL (empty)

456cdef void* __cuTensorMapEncodeIm2col = NULL (empty)

457cdef void* __cuTensorMapEncodeIm2colWide = NULL (empty)

458cdef void* __cuTensorMapReplaceAddress = NULL (empty)

459cdef void* __cuDeviceCanAccessPeer = NULL (empty)

460cdef void* __cuCtxEnablePeerAccess = NULL (empty)

461cdef void* __cuCtxDisablePeerAccess = NULL (empty)

462cdef void* __cuDeviceGetP2PAttribute = NULL (empty)

463cdef void* __cuGraphicsUnregisterResource = NULL (empty)

464cdef void* __cuGraphicsSubResourceGetMappedArray = NULL (empty)

465cdef void* __cuGraphicsResourceGetMappedMipmappedArray = NULL (empty)

466cdef void* __cuGraphicsResourceGetMappedPointer_v2 = NULL (empty)

467cdef void* __cuGraphicsResourceSetMapFlags_v2 = NULL (empty)

468cdef void* __cuGraphicsMapResources = NULL (empty)

469cdef void* __cuGraphicsUnmapResources = NULL (empty)

470cdef void* __cuGetProcAddress_v2 = NULL (empty)

471cdef void* __cuCoredumpGetAttribute = NULL (empty)

472cdef void* __cuCoredumpGetAttributeGlobal = NULL (empty)

473cdef void* __cuCoredumpSetAttribute = NULL (empty)

474cdef void* __cuCoredumpSetAttributeGlobal = NULL (empty)

475cdef void* __cuGetExportTable = NULL (empty)

476cdef void* __cuGreenCtxCreate = NULL (empty)

477cdef void* __cuGreenCtxDestroy = NULL (empty)

478cdef void* __cuCtxFromGreenCtx = NULL (empty)

479cdef void* __cuDeviceGetDevResource = NULL (empty)

480cdef void* __cuCtxGetDevResource = NULL (empty)

481cdef void* __cuGreenCtxGetDevResource = NULL (empty)

482cdef void* __cuDevSmResourceSplitByCount = NULL (empty)

483cdef void* __cuDevResourceGenerateDesc = NULL (empty)

484cdef void* __cuGreenCtxRecordEvent = NULL (empty)

485cdef void* __cuGreenCtxWaitEvent = NULL (empty)

486cdef void* __cuStreamGetGreenCtx = NULL (empty)

487cdef void* __cuGreenCtxStreamCreate = NULL (empty)

488cdef void* __cuLogsRegisterCallback = NULL (empty)

489cdef void* __cuLogsUnregisterCallback = NULL (empty)

490cdef void* __cuLogsCurrent = NULL (empty)

491cdef void* __cuLogsDumpToFile = NULL (empty)

492cdef void* __cuLogsDumpToMemory = NULL (empty)

493cdef void* __cuCheckpointProcessGetRestoreThreadId = NULL (empty)

494cdef void* __cuCheckpointProcessGetState = NULL (empty)

495cdef void* __cuCheckpointProcessLock = NULL (empty)

496cdef void* __cuCheckpointProcessCheckpoint = NULL (empty)

497cdef void* __cuCheckpointProcessRestore = NULL (empty)

498cdef void* __cuCheckpointProcessUnlock = NULL (empty)

499cdef void* __cuGraphicsEGLRegisterImage = NULL (empty)

500cdef void* __cuEGLStreamConsumerConnect = NULL (empty)

501cdef void* __cuEGLStreamConsumerConnectWithFlags = NULL (empty)

502cdef void* __cuEGLStreamConsumerDisconnect = NULL (empty)

503cdef void* __cuEGLStreamConsumerAcquireFrame = NULL (empty)

504cdef void* __cuEGLStreamConsumerReleaseFrame = NULL (empty)

505cdef void* __cuEGLStreamProducerConnect = NULL (empty)

506cdef void* __cuEGLStreamProducerDisconnect = NULL (empty)

507cdef void* __cuEGLStreamProducerPresentFrame = NULL (empty)

508cdef void* __cuEGLStreamProducerReturnFrame = NULL (empty)

509cdef void* __cuGraphicsResourceGetMappedEglFrame = NULL (empty)

510cdef void* __cuEventCreateFromEGLSync = NULL (empty)

511cdef void* __cuGraphicsGLRegisterBuffer = NULL (empty)

512cdef void* __cuGraphicsGLRegisterImage = NULL (empty)

513cdef void* __cuGLGetDevices_v2 = NULL (empty)

514cdef void* __cuGLCtxCreate_v2 = NULL (empty)

515cdef void* __cuGLInit = NULL (empty)

516cdef void* __cuGLRegisterBufferObject = NULL (empty)

517cdef void* __cuGLMapBufferObject_v2 = NULL (empty)

518cdef void* __cuGLUnmapBufferObject = NULL (empty)

519cdef void* __cuGLUnregisterBufferObject = NULL (empty)

520cdef void* __cuGLSetBufferObjectMapFlags = NULL (empty)

521cdef void* __cuGLMapBufferObjectAsync_v2 = NULL (empty)

522cdef void* __cuGLUnmapBufferObjectAsync = NULL (empty)

523cdef void* __cuProfilerInitialize = NULL (empty)

524cdef void* __cuProfilerStart = NULL (empty)

525cdef void* __cuProfilerStop = NULL (empty)

526cdef void* __cuVDPAUGetDevice = NULL (empty)

527cdef void* __cuVDPAUCtxCreate_v2 = NULL (empty)

528cdef void* __cuGraphicsVDPAURegisterVideoSurface = NULL (empty)

529cdef void* __cuGraphicsVDPAURegisterOutputSurface = NULL (empty)

530cdef void* __cuDeviceGetHostAtomicCapabilities = NULL (empty)

531cdef void* __cuCtxGetDevice_v2 = NULL (empty)

532cdef void* __cuCtxSynchronize_v2 = NULL (empty)

533cdef void* __cuMemcpyBatchAsync_v2 = NULL (empty)

534cdef void* __cuMemcpy3DBatchAsync_v2 = NULL (empty)

535cdef void* __cuMemGetDefaultMemPool = NULL (empty)

536cdef void* __cuMemGetMemPool = NULL (empty)

537cdef void* __cuMemSetMemPool = NULL (empty)

538cdef void* __cuMemPrefetchBatchAsync = NULL (empty)

539cdef void* __cuMemDiscardBatchAsync = NULL (empty)

540cdef void* __cuMemDiscardAndPrefetchBatchAsync = NULL (empty)

541cdef void* __cuDeviceGetP2PAtomicCapabilities = NULL (empty)

542cdef void* __cuGreenCtxGetId = NULL (empty)

543cdef void* __cuMulticastBindMem_v2 = NULL (empty)

544cdef void* __cuMulticastBindAddr_v2 = NULL (empty)

545cdef void* __cuGraphNodeGetContainingGraph = NULL (empty)

546cdef void* __cuGraphNodeGetLocalId = NULL (empty)

547cdef void* __cuGraphNodeGetToolsId = NULL (empty)

548cdef void* __cuGraphGetId = NULL (empty)

549cdef void* __cuGraphExecGetId = NULL (empty)

550cdef void* __cuDevSmResourceSplit = NULL (empty)

551cdef void* __cuStreamGetDevResource = NULL (empty)

552cdef void* __cuKernelGetParamCount = NULL (empty)

553cdef void* __cuMemcpyWithAttributesAsync = NULL (empty)

554cdef void* __cuMemcpy3DWithAttributesAsync = NULL (empty)

555cdef void* __cuStreamBeginCaptureToCig = NULL (empty)

556cdef void* __cuStreamEndCaptureToCig = NULL (empty)

557cdef void* __cuFuncGetParamCount = NULL (empty)

558cdef void* __cuLaunchHostFunc_v2 = NULL (empty)

559cdef void* __cuGraphNodeGetParams = NULL (empty)

560cdef void* __cuCoredumpRegisterStartCallback = NULL (empty)

561cdef void* __cuCoredumpRegisterCompleteCallback = NULL (empty)

562cdef void* __cuCoredumpDeregisterStartCallback = NULL (empty)

563cdef void* __cuCoredumpDeregisterCompleteCallback = NULL (empty)

564cdef void* __cuLogicalEndpointIdReserve = NULL (empty)

565cdef void* __cuLogicalEndpointIdRelease = NULL (empty)

566cdef void* __cuLogicalEndpointCreate = NULL (empty)

567cdef void* __cuLogicalEndpointAddDevice = NULL (empty)

568cdef void* __cuLogicalEndpointDestroy = NULL (empty)

569cdef void* __cuLogicalEndpointBindAddr = NULL (empty)

570cdef void* __cuLogicalEndpointBindMem = NULL (empty)

571cdef void* __cuLogicalEndpointUnbind = NULL (empty)

572cdef void* __cuLogicalEndpointExport = NULL (empty)

573cdef void* __cuLogicalEndpointImport = NULL (empty)

574cdef void* __cuLogicalEndpointGetLimits = NULL (empty)

575cdef void* __cuLogicalEndpointQuery = NULL (empty)

576cdef void* __cuStreamBeginRecaptureToGraph = NULL (empty)

577  

578  

579  

580cdef void* load_library() except* with gil: (empty)

581 cdef uintptr_t handle = load_nvidia_dynamic_lib("cuda")._handle_uint (empty)

582 return <void*>handle (empty)

583  

584  

585ctypedef CUresult (*__cuGetProcAddress_v2_T)(const char*, void**, int, cuuint64_t, CUdriverProcAddressQueryResult*) except?CUDA_ERROR_NOT_FOUND nogil 

586cdef __cuGetProcAddress_v2_T _F_cuGetProcAddress_v2 = NULL (empty)

587  

588  

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

590 global __py_driver_init 

591  

592 cdef void* handle = NULL (empty)

593 cdef int ptds_mode 

594  

595 with gil, __symbol_lock: (empty)

596 # Recheck the flag after obtaining the locks 

597 if __py_driver_init: (empty)

598 return 0 (empty)

599  

600 handle = load_library() (empty)

601 if handle == NULL: (empty)

602 raise RuntimeError('Failed to open cuda') 

603  

604 # Get latest __cuGetProcAddress_v2 

605 global __cuGetProcAddress_v2 

606 __cuGetProcAddress_v2 = dlsym(handle, 'cuGetProcAddress_v2') (empty)

607 if __cuGetProcAddress_v2 == NULL: (empty)

608 raise RuntimeError("Failed to get __cuGetProcAddress_v2") 

609 _F_cuGetProcAddress_v2 = <__cuGetProcAddress_v2_T>__cuGetProcAddress_v2 (empty)

610  

611 if bool(int(os.getenv('CUDA_PYTHON_CUDA_PER_THREAD_DEFAULT_STREAM', default=0))): (empty)

612 ptds_mode = CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM (empty)

613 else: 

614 ptds_mode = CU_GET_PROC_ADDRESS_DEFAULT (empty)

615  

616 # Load function 

617 global __cuGetErrorString 

618 _F_cuGetProcAddress_v2('cuGetErrorString', <void **>&__cuGetErrorString, 6000, ptds_mode, NULL) (empty)

619  

620 global __cuGetErrorName 

621 _F_cuGetProcAddress_v2('cuGetErrorName', <void **>&__cuGetErrorName, 6000, ptds_mode, NULL) (empty)

622  

623 global __cuInit 

624 _F_cuGetProcAddress_v2('cuInit', <void **>&__cuInit, 2000, ptds_mode, NULL) (empty)

625  

626 global __cuDriverGetVersion 

627 _F_cuGetProcAddress_v2('cuDriverGetVersion', <void **>&__cuDriverGetVersion, 2020, ptds_mode, NULL) (empty)

628  

629 global __cuDeviceGet 

630 _F_cuGetProcAddress_v2('cuDeviceGet', <void **>&__cuDeviceGet, 2000, ptds_mode, NULL) (empty)

631  

632 global __cuDeviceGetCount 

633 _F_cuGetProcAddress_v2('cuDeviceGetCount', <void **>&__cuDeviceGetCount, 2000, ptds_mode, NULL) (empty)

634  

635 global __cuDeviceGetName 

636 _F_cuGetProcAddress_v2('cuDeviceGetName', <void **>&__cuDeviceGetName, 2000, ptds_mode, NULL) (empty)

637  

638 global __cuDeviceGetUuid_v2 

639 _F_cuGetProcAddress_v2('cuDeviceGetUuid', <void **>&__cuDeviceGetUuid_v2, 11040, ptds_mode, NULL) (empty)

640  

641 global __cuDeviceGetLuid 

642 _F_cuGetProcAddress_v2('cuDeviceGetLuid', <void **>&__cuDeviceGetLuid, 10000, ptds_mode, NULL) (empty)

643  

644 global __cuDeviceTotalMem_v2 

645 _F_cuGetProcAddress_v2('cuDeviceTotalMem', <void **>&__cuDeviceTotalMem_v2, 3020, ptds_mode, NULL) (empty)

646  

647 global __cuDeviceGetTexture1DLinearMaxWidth 

648 _F_cuGetProcAddress_v2('cuDeviceGetTexture1DLinearMaxWidth', <void **>&__cuDeviceGetTexture1DLinearMaxWidth, 11010, ptds_mode, NULL) (empty)

649  

650 global __cuDeviceGetAttribute 

651 _F_cuGetProcAddress_v2('cuDeviceGetAttribute', <void **>&__cuDeviceGetAttribute, 2000, ptds_mode, NULL) (empty)

652  

653 global __cuDeviceGetNvSciSyncAttributes 

654 _F_cuGetProcAddress_v2('cuDeviceGetNvSciSyncAttributes', <void **>&__cuDeviceGetNvSciSyncAttributes, 10020, ptds_mode, NULL) (empty)

655  

656 global __cuDeviceSetMemPool 

657 _F_cuGetProcAddress_v2('cuDeviceSetMemPool', <void **>&__cuDeviceSetMemPool, 11020, ptds_mode, NULL) (empty)

658  

659 global __cuDeviceGetMemPool 

660 _F_cuGetProcAddress_v2('cuDeviceGetMemPool', <void **>&__cuDeviceGetMemPool, 11020, ptds_mode, NULL) (empty)

661  

662 global __cuDeviceGetDefaultMemPool 

663 _F_cuGetProcAddress_v2('cuDeviceGetDefaultMemPool', <void **>&__cuDeviceGetDefaultMemPool, 11020, ptds_mode, NULL) (empty)

664  

665 global __cuDeviceGetExecAffinitySupport 

666 _F_cuGetProcAddress_v2('cuDeviceGetExecAffinitySupport', <void **>&__cuDeviceGetExecAffinitySupport, 11040, ptds_mode, NULL) (empty)

667  

668 global __cuFlushGPUDirectRDMAWrites 

669 _F_cuGetProcAddress_v2('cuFlushGPUDirectRDMAWrites', <void **>&__cuFlushGPUDirectRDMAWrites, 11030, ptds_mode, NULL) (empty)

670  

671 global __cuDeviceGetProperties 

672 _F_cuGetProcAddress_v2('cuDeviceGetProperties', <void **>&__cuDeviceGetProperties, 2000, ptds_mode, NULL) (empty)

673  

674 global __cuDeviceComputeCapability 

675 _F_cuGetProcAddress_v2('cuDeviceComputeCapability', <void **>&__cuDeviceComputeCapability, 2000, ptds_mode, NULL) (empty)

676  

677 global __cuDevicePrimaryCtxRetain 

678 _F_cuGetProcAddress_v2('cuDevicePrimaryCtxRetain', <void **>&__cuDevicePrimaryCtxRetain, 7000, ptds_mode, NULL) (empty)

679  

680 global __cuDevicePrimaryCtxRelease_v2 

681 _F_cuGetProcAddress_v2('cuDevicePrimaryCtxRelease', <void **>&__cuDevicePrimaryCtxRelease_v2, 11000, ptds_mode, NULL) (empty)

682  

683 global __cuDevicePrimaryCtxSetFlags_v2 

684 _F_cuGetProcAddress_v2('cuDevicePrimaryCtxSetFlags', <void **>&__cuDevicePrimaryCtxSetFlags_v2, 11000, ptds_mode, NULL) (empty)

685  

686 global __cuDevicePrimaryCtxGetState 

687 _F_cuGetProcAddress_v2('cuDevicePrimaryCtxGetState', <void **>&__cuDevicePrimaryCtxGetState, 7000, ptds_mode, NULL) (empty)

688  

689 global __cuDevicePrimaryCtxReset_v2 

690 _F_cuGetProcAddress_v2('cuDevicePrimaryCtxReset', <void **>&__cuDevicePrimaryCtxReset_v2, 11000, ptds_mode, NULL) (empty)

691  

692 global __cuCtxCreate_v4 

693 _F_cuGetProcAddress_v2('cuCtxCreate', <void **>&__cuCtxCreate_v4, 12050, ptds_mode, NULL) (empty)

694  

695 global __cuCtxDestroy_v2 

696 _F_cuGetProcAddress_v2('cuCtxDestroy', <void **>&__cuCtxDestroy_v2, 4000, ptds_mode, NULL) (empty)

697  

698 global __cuCtxPushCurrent_v2 

699 _F_cuGetProcAddress_v2('cuCtxPushCurrent', <void **>&__cuCtxPushCurrent_v2, 4000, ptds_mode, NULL) (empty)

700  

701 global __cuCtxPopCurrent_v2 

702 _F_cuGetProcAddress_v2('cuCtxPopCurrent', <void **>&__cuCtxPopCurrent_v2, 4000, ptds_mode, NULL) (empty)

703  

704 global __cuCtxSetCurrent 

705 _F_cuGetProcAddress_v2('cuCtxSetCurrent', <void **>&__cuCtxSetCurrent, 4000, ptds_mode, NULL) (empty)

706  

707 global __cuCtxGetCurrent 

708 _F_cuGetProcAddress_v2('cuCtxGetCurrent', <void **>&__cuCtxGetCurrent, 4000, ptds_mode, NULL) (empty)

709  

710 global __cuCtxGetDevice 

711 _F_cuGetProcAddress_v2('cuCtxGetDevice', <void **>&__cuCtxGetDevice, 2000, ptds_mode, NULL) (empty)

712  

713 global __cuCtxGetFlags 

714 _F_cuGetProcAddress_v2('cuCtxGetFlags', <void **>&__cuCtxGetFlags, 7000, ptds_mode, NULL) (empty)

715  

716 global __cuCtxSetFlags 

717 _F_cuGetProcAddress_v2('cuCtxSetFlags', <void **>&__cuCtxSetFlags, 12010, ptds_mode, NULL) (empty)

718  

719 global __cuCtxGetId 

720 _F_cuGetProcAddress_v2('cuCtxGetId', <void **>&__cuCtxGetId, 12000, ptds_mode, NULL) (empty)

721  

722 global __cuCtxSynchronize 

723 _F_cuGetProcAddress_v2('cuCtxSynchronize', <void **>&__cuCtxSynchronize, 2000, ptds_mode, NULL) (empty)

724  

725 global __cuCtxSetLimit 

726 _F_cuGetProcAddress_v2('cuCtxSetLimit', <void **>&__cuCtxSetLimit, 3010, ptds_mode, NULL) (empty)

727  

728 global __cuCtxGetLimit 

729 _F_cuGetProcAddress_v2('cuCtxGetLimit', <void **>&__cuCtxGetLimit, 3010, ptds_mode, NULL) (empty)

730  

731 global __cuCtxGetCacheConfig 

732 _F_cuGetProcAddress_v2('cuCtxGetCacheConfig', <void **>&__cuCtxGetCacheConfig, 3020, ptds_mode, NULL) (empty)

733  

734 global __cuCtxSetCacheConfig 

735 _F_cuGetProcAddress_v2('cuCtxSetCacheConfig', <void **>&__cuCtxSetCacheConfig, 3020, ptds_mode, NULL) (empty)

736  

737 global __cuCtxGetApiVersion 

738 _F_cuGetProcAddress_v2('cuCtxGetApiVersion', <void **>&__cuCtxGetApiVersion, 3020, ptds_mode, NULL) (empty)

739  

740 global __cuCtxGetStreamPriorityRange 

741 _F_cuGetProcAddress_v2('cuCtxGetStreamPriorityRange', <void **>&__cuCtxGetStreamPriorityRange, 5050, ptds_mode, NULL) (empty)

742  

743 global __cuCtxResetPersistingL2Cache 

744 _F_cuGetProcAddress_v2('cuCtxResetPersistingL2Cache', <void **>&__cuCtxResetPersistingL2Cache, 11000, ptds_mode, NULL) (empty)

745  

746 global __cuCtxGetExecAffinity 

747 _F_cuGetProcAddress_v2('cuCtxGetExecAffinity', <void **>&__cuCtxGetExecAffinity, 11040, ptds_mode, NULL) (empty)

748  

749 global __cuCtxRecordEvent 

750 _F_cuGetProcAddress_v2('cuCtxRecordEvent', <void **>&__cuCtxRecordEvent, 12050, ptds_mode, NULL) (empty)

751  

752 global __cuCtxWaitEvent 

753 _F_cuGetProcAddress_v2('cuCtxWaitEvent', <void **>&__cuCtxWaitEvent, 12050, ptds_mode, NULL) (empty)

754  

755 global __cuCtxAttach 

756 _F_cuGetProcAddress_v2('cuCtxAttach', <void **>&__cuCtxAttach, 2000, ptds_mode, NULL) (empty)

757  

758 global __cuCtxDetach 

759 _F_cuGetProcAddress_v2('cuCtxDetach', <void **>&__cuCtxDetach, 2000, ptds_mode, NULL) (empty)

760  

761 global __cuCtxGetSharedMemConfig 

762 _F_cuGetProcAddress_v2('cuCtxGetSharedMemConfig', <void **>&__cuCtxGetSharedMemConfig, 4020, ptds_mode, NULL) (empty)

763  

764 global __cuCtxSetSharedMemConfig 

765 _F_cuGetProcAddress_v2('cuCtxSetSharedMemConfig', <void **>&__cuCtxSetSharedMemConfig, 4020, ptds_mode, NULL) (empty)

766  

767 global __cuModuleLoad 

768 _F_cuGetProcAddress_v2('cuModuleLoad', <void **>&__cuModuleLoad, 2000, ptds_mode, NULL) (empty)

769  

770 global __cuModuleLoadData 

771 _F_cuGetProcAddress_v2('cuModuleLoadData', <void **>&__cuModuleLoadData, 2000, ptds_mode, NULL) (empty)

772  

773 global __cuModuleLoadDataEx 

774 _F_cuGetProcAddress_v2('cuModuleLoadDataEx', <void **>&__cuModuleLoadDataEx, 2010, ptds_mode, NULL) (empty)

775  

776 global __cuModuleLoadFatBinary 

777 _F_cuGetProcAddress_v2('cuModuleLoadFatBinary', <void **>&__cuModuleLoadFatBinary, 2000, ptds_mode, NULL) (empty)

778  

779 global __cuModuleUnload 

780 _F_cuGetProcAddress_v2('cuModuleUnload', <void **>&__cuModuleUnload, 2000, ptds_mode, NULL) (empty)

781  

782 global __cuModuleGetLoadingMode 

783 _F_cuGetProcAddress_v2('cuModuleGetLoadingMode', <void **>&__cuModuleGetLoadingMode, 11070, ptds_mode, NULL) (empty)

784  

785 global __cuModuleGetFunction 

786 _F_cuGetProcAddress_v2('cuModuleGetFunction', <void **>&__cuModuleGetFunction, 2000, ptds_mode, NULL) (empty)

787  

788 global __cuModuleGetFunctionCount 

789 _F_cuGetProcAddress_v2('cuModuleGetFunctionCount', <void **>&__cuModuleGetFunctionCount, 12040, ptds_mode, NULL) (empty)

790  

791 global __cuModuleEnumerateFunctions 

792 _F_cuGetProcAddress_v2('cuModuleEnumerateFunctions', <void **>&__cuModuleEnumerateFunctions, 12040, ptds_mode, NULL) (empty)

793  

794 global __cuModuleGetGlobal_v2 

795 _F_cuGetProcAddress_v2('cuModuleGetGlobal', <void **>&__cuModuleGetGlobal_v2, 3020, ptds_mode, NULL) (empty)

796  

797 global __cuLinkCreate_v2 

798 _F_cuGetProcAddress_v2('cuLinkCreate', <void **>&__cuLinkCreate_v2, 6050, ptds_mode, NULL) (empty)

799  

800 global __cuLinkAddData_v2 

801 _F_cuGetProcAddress_v2('cuLinkAddData', <void **>&__cuLinkAddData_v2, 6050, ptds_mode, NULL) (empty)

802  

803 global __cuLinkAddFile_v2 

804 _F_cuGetProcAddress_v2('cuLinkAddFile', <void **>&__cuLinkAddFile_v2, 6050, ptds_mode, NULL) (empty)

805  

806 global __cuLinkComplete 

807 _F_cuGetProcAddress_v2('cuLinkComplete', <void **>&__cuLinkComplete, 5050, ptds_mode, NULL) (empty)

808  

809 global __cuLinkDestroy 

810 _F_cuGetProcAddress_v2('cuLinkDestroy', <void **>&__cuLinkDestroy, 5050, ptds_mode, NULL) (empty)

811  

812 global __cuModuleGetTexRef 

813 _F_cuGetProcAddress_v2('cuModuleGetTexRef', <void **>&__cuModuleGetTexRef, 2000, ptds_mode, NULL) (empty)

814  

815 global __cuModuleGetSurfRef 

816 _F_cuGetProcAddress_v2('cuModuleGetSurfRef', <void **>&__cuModuleGetSurfRef, 3000, ptds_mode, NULL) (empty)

817  

818 global __cuLibraryLoadData 

819 _F_cuGetProcAddress_v2('cuLibraryLoadData', <void **>&__cuLibraryLoadData, 12000, ptds_mode, NULL) (empty)

820  

821 global __cuLibraryLoadFromFile 

822 _F_cuGetProcAddress_v2('cuLibraryLoadFromFile', <void **>&__cuLibraryLoadFromFile, 12000, ptds_mode, NULL) (empty)

823  

824 global __cuLibraryUnload 

825 _F_cuGetProcAddress_v2('cuLibraryUnload', <void **>&__cuLibraryUnload, 12000, ptds_mode, NULL) (empty)

826  

827 global __cuLibraryGetKernel 

828 _F_cuGetProcAddress_v2('cuLibraryGetKernel', <void **>&__cuLibraryGetKernel, 12000, ptds_mode, NULL) (empty)

829  

830 global __cuLibraryGetKernelCount 

831 _F_cuGetProcAddress_v2('cuLibraryGetKernelCount', <void **>&__cuLibraryGetKernelCount, 12040, ptds_mode, NULL) (empty)

832  

833 global __cuLibraryEnumerateKernels 

834 _F_cuGetProcAddress_v2('cuLibraryEnumerateKernels', <void **>&__cuLibraryEnumerateKernels, 12040, ptds_mode, NULL) (empty)

835  

836 global __cuLibraryGetModule 

837 _F_cuGetProcAddress_v2('cuLibraryGetModule', <void **>&__cuLibraryGetModule, 12000, ptds_mode, NULL) (empty)

838  

839 global __cuKernelGetFunction 

840 _F_cuGetProcAddress_v2('cuKernelGetFunction', <void **>&__cuKernelGetFunction, 12000, ptds_mode, NULL) (empty)

841  

842 global __cuKernelGetLibrary 

843 _F_cuGetProcAddress_v2('cuKernelGetLibrary', <void **>&__cuKernelGetLibrary, 12050, ptds_mode, NULL) (empty)

844  

845 global __cuLibraryGetGlobal 

846 _F_cuGetProcAddress_v2('cuLibraryGetGlobal', <void **>&__cuLibraryGetGlobal, 12000, ptds_mode, NULL) (empty)

847  

848 global __cuLibraryGetManaged 

849 _F_cuGetProcAddress_v2('cuLibraryGetManaged', <void **>&__cuLibraryGetManaged, 12000, ptds_mode, NULL) (empty)

850  

851 global __cuLibraryGetUnifiedFunction 

852 _F_cuGetProcAddress_v2('cuLibraryGetUnifiedFunction', <void **>&__cuLibraryGetUnifiedFunction, 12000, ptds_mode, NULL) (empty)

853  

854 global __cuKernelGetAttribute 

855 _F_cuGetProcAddress_v2('cuKernelGetAttribute', <void **>&__cuKernelGetAttribute, 12000, ptds_mode, NULL) (empty)

856  

857 global __cuKernelSetAttribute 

858 _F_cuGetProcAddress_v2('cuKernelSetAttribute', <void **>&__cuKernelSetAttribute, 12000, ptds_mode, NULL) (empty)

859  

860 global __cuKernelSetCacheConfig 

861 _F_cuGetProcAddress_v2('cuKernelSetCacheConfig', <void **>&__cuKernelSetCacheConfig, 12000, ptds_mode, NULL) (empty)

862  

863 global __cuKernelGetName 

864 _F_cuGetProcAddress_v2('cuKernelGetName', <void **>&__cuKernelGetName, 12030, ptds_mode, NULL) (empty)

865  

866 global __cuKernelGetParamInfo 

867 _F_cuGetProcAddress_v2('cuKernelGetParamInfo', <void **>&__cuKernelGetParamInfo, 12040, ptds_mode, NULL) (empty)

868  

869 global __cuMemGetInfo_v2 

870 _F_cuGetProcAddress_v2('cuMemGetInfo', <void **>&__cuMemGetInfo_v2, 3020, ptds_mode, NULL) (empty)

871  

872 global __cuMemAlloc_v2 

873 _F_cuGetProcAddress_v2('cuMemAlloc', <void **>&__cuMemAlloc_v2, 3020, ptds_mode, NULL) (empty)

874  

875 global __cuMemAllocPitch_v2 

876 _F_cuGetProcAddress_v2('cuMemAllocPitch', <void **>&__cuMemAllocPitch_v2, 3020, ptds_mode, NULL) (empty)

877  

878 global __cuMemFree_v2 

879 _F_cuGetProcAddress_v2('cuMemFree', <void **>&__cuMemFree_v2, 3020, ptds_mode, NULL) (empty)

880  

881 global __cuMemGetAddressRange_v2 

882 _F_cuGetProcAddress_v2('cuMemGetAddressRange', <void **>&__cuMemGetAddressRange_v2, 3020, ptds_mode, NULL) (empty)

883  

884 global __cuMemAllocHost_v2 

885 _F_cuGetProcAddress_v2('cuMemAllocHost', <void **>&__cuMemAllocHost_v2, 3020, ptds_mode, NULL) (empty)

886  

887 global __cuMemFreeHost 

888 _F_cuGetProcAddress_v2('cuMemFreeHost', <void **>&__cuMemFreeHost, 2000, ptds_mode, NULL) (empty)

889  

890 global __cuMemHostAlloc 

891 _F_cuGetProcAddress_v2('cuMemHostAlloc', <void **>&__cuMemHostAlloc, 2020, ptds_mode, NULL) (empty)

892  

893 global __cuMemHostGetDevicePointer_v2 

894 _F_cuGetProcAddress_v2('cuMemHostGetDevicePointer', <void **>&__cuMemHostGetDevicePointer_v2, 3020, ptds_mode, NULL) (empty)

895  

896 global __cuMemHostGetFlags 

897 _F_cuGetProcAddress_v2('cuMemHostGetFlags', <void **>&__cuMemHostGetFlags, 2030, ptds_mode, NULL) (empty)

898  

899 global __cuMemAllocManaged 

900 _F_cuGetProcAddress_v2('cuMemAllocManaged', <void **>&__cuMemAllocManaged, 6000, ptds_mode, NULL) (empty)

901  

902 global __cuDeviceRegisterAsyncNotification 

903 _F_cuGetProcAddress_v2('cuDeviceRegisterAsyncNotification', <void **>&__cuDeviceRegisterAsyncNotification, 12040, ptds_mode, NULL) (empty)

904  

905 global __cuDeviceUnregisterAsyncNotification 

906 _F_cuGetProcAddress_v2('cuDeviceUnregisterAsyncNotification', <void **>&__cuDeviceUnregisterAsyncNotification, 12040, ptds_mode, NULL) (empty)

907  

908 global __cuDeviceGetByPCIBusId 

909 _F_cuGetProcAddress_v2('cuDeviceGetByPCIBusId', <void **>&__cuDeviceGetByPCIBusId, 4010, ptds_mode, NULL) (empty)

910  

911 global __cuDeviceGetPCIBusId 

912 _F_cuGetProcAddress_v2('cuDeviceGetPCIBusId', <void **>&__cuDeviceGetPCIBusId, 4010, ptds_mode, NULL) (empty)

913  

914 global __cuIpcGetEventHandle 

915 _F_cuGetProcAddress_v2('cuIpcGetEventHandle', <void **>&__cuIpcGetEventHandle, 4010, ptds_mode, NULL) (empty)

916  

917 global __cuIpcOpenEventHandle 

918 _F_cuGetProcAddress_v2('cuIpcOpenEventHandle', <void **>&__cuIpcOpenEventHandle, 4010, ptds_mode, NULL) (empty)

919  

920 global __cuIpcGetMemHandle 

921 _F_cuGetProcAddress_v2('cuIpcGetMemHandle', <void **>&__cuIpcGetMemHandle, 4010, ptds_mode, NULL) (empty)

922  

923 global __cuIpcOpenMemHandle_v2 

924 _F_cuGetProcAddress_v2('cuIpcOpenMemHandle', <void **>&__cuIpcOpenMemHandle_v2, 11000, ptds_mode, NULL) (empty)

925  

926 global __cuIpcCloseMemHandle 

927 _F_cuGetProcAddress_v2('cuIpcCloseMemHandle', <void **>&__cuIpcCloseMemHandle, 4010, ptds_mode, NULL) (empty)

928  

929 global __cuMemHostRegister_v2 

930 _F_cuGetProcAddress_v2('cuMemHostRegister', <void **>&__cuMemHostRegister_v2, 6050, ptds_mode, NULL) (empty)

931  

932 global __cuMemHostUnregister 

933 _F_cuGetProcAddress_v2('cuMemHostUnregister', <void **>&__cuMemHostUnregister, 4000, ptds_mode, NULL) (empty)

934  

935 global __cuMemcpy 

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

937  

938 global __cuMemcpyPeer 

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

940  

941 global __cuMemcpyHtoD_v2 

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

943  

944 global __cuMemcpyDtoH_v2 

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

946  

947 global __cuMemcpyDtoD_v2 

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

949  

950 global __cuMemcpyDtoA_v2 

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

952  

953 global __cuMemcpyAtoD_v2 

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

955  

956 global __cuMemcpyHtoA_v2 

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

958  

959 global __cuMemcpyAtoH_v2 

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

961  

962 global __cuMemcpyAtoA_v2 

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

964  

965 global __cuMemcpy2D_v2 

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

967  

968 global __cuMemcpy2DUnaligned_v2 

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

970  

971 global __cuMemcpy3D_v2 

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

973  

974 global __cuMemcpy3DPeer 

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

976  

977 global __cuMemcpyAsync 

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

979  

980 global __cuMemcpyPeerAsync 

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

982  

983 global __cuMemcpyHtoDAsync_v2 

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

985  

986 global __cuMemcpyDtoHAsync_v2 

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

988  

989 global __cuMemcpyDtoDAsync_v2 

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

991  

992 global __cuMemcpyHtoAAsync_v2 

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

994  

995 global __cuMemcpyAtoHAsync_v2 

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

997  

998 global __cuMemcpy2DAsync_v2 

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

1000  

1001 global __cuMemcpy3DAsync_v2 

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

1003  

1004 global __cuMemcpy3DPeerAsync 

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

1006  

1007 global __cuMemsetD8_v2 

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

1009  

1010 global __cuMemsetD16_v2 

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

1012  

1013 global __cuMemsetD32_v2 

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

1015  

1016 global __cuMemsetD2D8_v2 

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

1018  

1019 global __cuMemsetD2D16_v2 

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

1021  

1022 global __cuMemsetD2D32_v2 

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

1024  

1025 global __cuMemsetD8Async 

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

1027  

1028 global __cuMemsetD16Async 

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

1030  

1031 global __cuMemsetD32Async 

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

1033  

1034 global __cuMemsetD2D8Async 

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

1036  

1037 global __cuMemsetD2D16Async 

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

1039  

1040 global __cuMemsetD2D32Async 

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

1042  

1043 global __cuArrayCreate_v2 

1044 _F_cuGetProcAddress_v2('cuArrayCreate', <void **>&__cuArrayCreate_v2, 3020, ptds_mode, NULL) (empty)

1045  

1046 global __cuArrayGetDescriptor_v2 

1047 _F_cuGetProcAddress_v2('cuArrayGetDescriptor', <void **>&__cuArrayGetDescriptor_v2, 3020, ptds_mode, NULL) (empty)

1048  

1049 global __cuArrayGetSparseProperties 

1050 _F_cuGetProcAddress_v2('cuArrayGetSparseProperties', <void **>&__cuArrayGetSparseProperties, 11010, ptds_mode, NULL) (empty)

1051  

1052 global __cuMipmappedArrayGetSparseProperties 

1053 _F_cuGetProcAddress_v2('cuMipmappedArrayGetSparseProperties', <void **>&__cuMipmappedArrayGetSparseProperties, 11010, ptds_mode, NULL) (empty)

1054  

1055 global __cuArrayGetMemoryRequirements 

1056 _F_cuGetProcAddress_v2('cuArrayGetMemoryRequirements', <void **>&__cuArrayGetMemoryRequirements, 11060, ptds_mode, NULL) (empty)

1057  

1058 global __cuMipmappedArrayGetMemoryRequirements 

1059 _F_cuGetProcAddress_v2('cuMipmappedArrayGetMemoryRequirements', <void **>&__cuMipmappedArrayGetMemoryRequirements, 11060, ptds_mode, NULL) (empty)

1060  

1061 global __cuArrayGetPlane 

1062 _F_cuGetProcAddress_v2('cuArrayGetPlane', <void **>&__cuArrayGetPlane, 11020, ptds_mode, NULL) (empty)

1063  

1064 global __cuArrayDestroy 

1065 _F_cuGetProcAddress_v2('cuArrayDestroy', <void **>&__cuArrayDestroy, 2000, ptds_mode, NULL) (empty)

1066  

1067 global __cuArray3DCreate_v2 

1068 _F_cuGetProcAddress_v2('cuArray3DCreate', <void **>&__cuArray3DCreate_v2, 3020, ptds_mode, NULL) (empty)

1069  

1070 global __cuArray3DGetDescriptor_v2 

1071 _F_cuGetProcAddress_v2('cuArray3DGetDescriptor', <void **>&__cuArray3DGetDescriptor_v2, 3020, ptds_mode, NULL) (empty)

1072  

1073 global __cuMipmappedArrayCreate 

1074 _F_cuGetProcAddress_v2('cuMipmappedArrayCreate', <void **>&__cuMipmappedArrayCreate, 5000, ptds_mode, NULL) (empty)

1075  

1076 global __cuMipmappedArrayGetLevel 

1077 _F_cuGetProcAddress_v2('cuMipmappedArrayGetLevel', <void **>&__cuMipmappedArrayGetLevel, 5000, ptds_mode, NULL) (empty)

1078  

1079 global __cuMipmappedArrayDestroy 

1080 _F_cuGetProcAddress_v2('cuMipmappedArrayDestroy', <void **>&__cuMipmappedArrayDestroy, 5000, ptds_mode, NULL) (empty)

1081  

1082 global __cuMemGetHandleForAddressRange 

1083 _F_cuGetProcAddress_v2('cuMemGetHandleForAddressRange', <void **>&__cuMemGetHandleForAddressRange, 11070, ptds_mode, NULL) (empty)

1084  

1085 global __cuMemBatchDecompressAsync 

1086 _F_cuGetProcAddress_v2('cuMemBatchDecompressAsync', <void **>&__cuMemBatchDecompressAsync, 12060, ptds_mode, NULL) (empty)

1087  

1088 global __cuMemAddressReserve 

1089 _F_cuGetProcAddress_v2('cuMemAddressReserve', <void **>&__cuMemAddressReserve, 10020, ptds_mode, NULL) (empty)

1090  

1091 global __cuMemAddressFree 

1092 _F_cuGetProcAddress_v2('cuMemAddressFree', <void **>&__cuMemAddressFree, 10020, ptds_mode, NULL) (empty)

1093  

1094 global __cuMemCreate 

1095 _F_cuGetProcAddress_v2('cuMemCreate', <void **>&__cuMemCreate, 10020, ptds_mode, NULL) (empty)

1096  

1097 global __cuMemRelease 

1098 _F_cuGetProcAddress_v2('cuMemRelease', <void **>&__cuMemRelease, 10020, ptds_mode, NULL) (empty)

1099  

1100 global __cuMemMap 

1101 _F_cuGetProcAddress_v2('cuMemMap', <void **>&__cuMemMap, 10020, ptds_mode, NULL) (empty)

1102  

1103 global __cuMemMapArrayAsync 

1104 _F_cuGetProcAddress_v2('cuMemMapArrayAsync', <void **>&__cuMemMapArrayAsync, 11010, ptds_mode, NULL) (empty)

1105  

1106 global __cuMemUnmap 

1107 _F_cuGetProcAddress_v2('cuMemUnmap', <void **>&__cuMemUnmap, 10020, ptds_mode, NULL) (empty)

1108  

1109 global __cuMemSetAccess 

1110 _F_cuGetProcAddress_v2('cuMemSetAccess', <void **>&__cuMemSetAccess, 10020, ptds_mode, NULL) (empty)

1111  

1112 global __cuMemGetAccess 

1113 _F_cuGetProcAddress_v2('cuMemGetAccess', <void **>&__cuMemGetAccess, 10020, ptds_mode, NULL) (empty)

1114  

1115 global __cuMemExportToShareableHandle 

1116 _F_cuGetProcAddress_v2('cuMemExportToShareableHandle', <void **>&__cuMemExportToShareableHandle, 10020, ptds_mode, NULL) (empty)

1117  

1118 global __cuMemImportFromShareableHandle 

1119 _F_cuGetProcAddress_v2('cuMemImportFromShareableHandle', <void **>&__cuMemImportFromShareableHandle, 10020, ptds_mode, NULL) (empty)

1120  

1121 global __cuMemGetAllocationGranularity 

1122 _F_cuGetProcAddress_v2('cuMemGetAllocationGranularity', <void **>&__cuMemGetAllocationGranularity, 10020, ptds_mode, NULL) (empty)

1123  

1124 global __cuMemGetAllocationPropertiesFromHandle 

1125 _F_cuGetProcAddress_v2('cuMemGetAllocationPropertiesFromHandle', <void **>&__cuMemGetAllocationPropertiesFromHandle, 10020, ptds_mode, NULL) (empty)

1126  

1127 global __cuMemRetainAllocationHandle 

1128 _F_cuGetProcAddress_v2('cuMemRetainAllocationHandle', <void **>&__cuMemRetainAllocationHandle, 11000, ptds_mode, NULL) (empty)

1129  

1130 global __cuMemFreeAsync 

1131 _F_cuGetProcAddress_v2('cuMemFreeAsync', <void **>&__cuMemFreeAsync, 11020, ptds_mode, NULL) (empty)

1132  

1133 global __cuMemAllocAsync 

1134 _F_cuGetProcAddress_v2('cuMemAllocAsync', <void **>&__cuMemAllocAsync, 11020, ptds_mode, NULL) (empty)

1135  

1136 global __cuMemPoolTrimTo 

1137 _F_cuGetProcAddress_v2('cuMemPoolTrimTo', <void **>&__cuMemPoolTrimTo, 11020, ptds_mode, NULL) (empty)

1138  

1139 global __cuMemPoolSetAttribute 

1140 _F_cuGetProcAddress_v2('cuMemPoolSetAttribute', <void **>&__cuMemPoolSetAttribute, 11020, ptds_mode, NULL) (empty)

1141  

1142 global __cuMemPoolGetAttribute 

1143 _F_cuGetProcAddress_v2('cuMemPoolGetAttribute', <void **>&__cuMemPoolGetAttribute, 11020, ptds_mode, NULL) (empty)

1144  

1145 global __cuMemPoolSetAccess 

1146 _F_cuGetProcAddress_v2('cuMemPoolSetAccess', <void **>&__cuMemPoolSetAccess, 11020, ptds_mode, NULL) (empty)

1147  

1148 global __cuMemPoolGetAccess 

1149 _F_cuGetProcAddress_v2('cuMemPoolGetAccess', <void **>&__cuMemPoolGetAccess, 11020, ptds_mode, NULL) (empty)

1150  

1151 global __cuMemPoolCreate 

1152 _F_cuGetProcAddress_v2('cuMemPoolCreate', <void **>&__cuMemPoolCreate, 11020, ptds_mode, NULL) (empty)

1153  

1154 global __cuMemPoolDestroy 

1155 _F_cuGetProcAddress_v2('cuMemPoolDestroy', <void **>&__cuMemPoolDestroy, 11020, ptds_mode, NULL) (empty)

1156  

1157 global __cuMemAllocFromPoolAsync 

1158 _F_cuGetProcAddress_v2('cuMemAllocFromPoolAsync', <void **>&__cuMemAllocFromPoolAsync, 11020, ptds_mode, NULL) (empty)

1159  

1160 global __cuMemPoolExportToShareableHandle 

1161 _F_cuGetProcAddress_v2('cuMemPoolExportToShareableHandle', <void **>&__cuMemPoolExportToShareableHandle, 11020, ptds_mode, NULL) (empty)

1162  

1163 global __cuMemPoolImportFromShareableHandle 

1164 _F_cuGetProcAddress_v2('cuMemPoolImportFromShareableHandle', <void **>&__cuMemPoolImportFromShareableHandle, 11020, ptds_mode, NULL) (empty)

1165  

1166 global __cuMemPoolExportPointer 

1167 _F_cuGetProcAddress_v2('cuMemPoolExportPointer', <void **>&__cuMemPoolExportPointer, 11020, ptds_mode, NULL) (empty)

1168  

1169 global __cuMemPoolImportPointer 

1170 _F_cuGetProcAddress_v2('cuMemPoolImportPointer', <void **>&__cuMemPoolImportPointer, 11020, ptds_mode, NULL) (empty)

1171  

1172 global __cuMulticastCreate 

1173 _F_cuGetProcAddress_v2('cuMulticastCreate', <void **>&__cuMulticastCreate, 12010, ptds_mode, NULL) (empty)

1174  

1175 global __cuMulticastAddDevice 

1176 _F_cuGetProcAddress_v2('cuMulticastAddDevice', <void **>&__cuMulticastAddDevice, 12010, ptds_mode, NULL) (empty)

1177  

1178 global __cuMulticastBindMem 

1179 _F_cuGetProcAddress_v2('cuMulticastBindMem', <void **>&__cuMulticastBindMem, 12010, ptds_mode, NULL) (empty)

1180  

1181 global __cuMulticastBindAddr 

1182 _F_cuGetProcAddress_v2('cuMulticastBindAddr', <void **>&__cuMulticastBindAddr, 12010, ptds_mode, NULL) (empty)

1183  

1184 global __cuMulticastUnbind 

1185 _F_cuGetProcAddress_v2('cuMulticastUnbind', <void **>&__cuMulticastUnbind, 12010, ptds_mode, NULL) (empty)

1186  

1187 global __cuMulticastGetGranularity 

1188 _F_cuGetProcAddress_v2('cuMulticastGetGranularity', <void **>&__cuMulticastGetGranularity, 12010, ptds_mode, NULL) (empty)

1189  

1190 global __cuPointerGetAttribute 

1191 _F_cuGetProcAddress_v2('cuPointerGetAttribute', <void **>&__cuPointerGetAttribute, 4000, ptds_mode, NULL) (empty)

1192  

1193 global __cuMemPrefetchAsync_v2 

1194 _F_cuGetProcAddress_v2('cuMemPrefetchAsync', <void **>&__cuMemPrefetchAsync_v2, 12020, ptds_mode, NULL) (empty)

1195  

1196 global __cuMemAdvise_v2 

1197 _F_cuGetProcAddress_v2('cuMemAdvise', <void **>&__cuMemAdvise_v2, 12020, ptds_mode, NULL) (empty)

1198  

1199 global __cuMemRangeGetAttribute 

1200 _F_cuGetProcAddress_v2('cuMemRangeGetAttribute', <void **>&__cuMemRangeGetAttribute, 8000, ptds_mode, NULL) (empty)

1201  

1202 global __cuMemRangeGetAttributes 

1203 _F_cuGetProcAddress_v2('cuMemRangeGetAttributes', <void **>&__cuMemRangeGetAttributes, 8000, ptds_mode, NULL) (empty)

1204  

1205 global __cuPointerSetAttribute 

1206 _F_cuGetProcAddress_v2('cuPointerSetAttribute', <void **>&__cuPointerSetAttribute, 6000, ptds_mode, NULL) (empty)

1207  

1208 global __cuPointerGetAttributes 

1209 _F_cuGetProcAddress_v2('cuPointerGetAttributes', <void **>&__cuPointerGetAttributes, 7000, ptds_mode, NULL) (empty)

1210  

1211 global __cuStreamCreate