Coverage for cuda/bindings/_internal/runtime_ptds.pyx: 50.08%

641 statements  

« prev     ^ index     » next       coverage.py v7.15.2, created at 2026-07-19 01:12 +0000

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

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  

7# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=33b0c77f7174d41189a91abfe73613b5ba48bd31b5da37d509da61c00b11a004 

8cdef extern from "": 

9 """ 

10 #define CUDA_API_PER_THREAD_DEFAULT_STREAM 

11 """ 

12  

13  

14############################################################################### 

15# C function declarations for static cudart with per-thread default stream 

16# (CUDA_API_PER_THREAD_DEFAULT_STREAM causes cudaXxx to resolve to the _ptsz 

17# per-thread-stream symbol variants) 

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

19  

20cdef extern from 'cuda_runtime_api.h' nogil: 

21 cudaError_t _static_cudaDeviceReset "cudaDeviceReset" () noexcept 

22  

23cdef extern from 'cuda_runtime_api.h' nogil: 

24 cudaError_t _static_cudaDeviceSynchronize "cudaDeviceSynchronize" () noexcept 

25  

26cdef extern from 'cuda_runtime_api.h' nogil: 

27 cudaError_t _static_cudaDeviceSetLimit "cudaDeviceSetLimit" (cudaLimit limit, size_t value) noexcept 

28  

29cdef extern from 'cuda_runtime_api.h' nogil: 

30 cudaError_t _static_cudaDeviceGetLimit "cudaDeviceGetLimit" (size_t* pValue, cudaLimit limit) noexcept 

31  

32cdef extern from 'cuda_runtime_api.h' nogil: 

33 cudaError_t _static_cudaDeviceGetTexture1DLinearMaxWidth "cudaDeviceGetTexture1DLinearMaxWidth" (size_t* maxWidthInElements, const cudaChannelFormatDesc* fmtDesc, int device) noexcept 

34  

35cdef extern from 'cuda_runtime_api.h' nogil: 

36 cudaError_t _static_cudaDeviceGetCacheConfig "cudaDeviceGetCacheConfig" (cudaFuncCache* pCacheConfig) noexcept 

37  

38cdef extern from 'cuda_runtime_api.h' nogil: 

39 cudaError_t _static_cudaDeviceGetStreamPriorityRange "cudaDeviceGetStreamPriorityRange" (int* leastPriority, int* greatestPriority) noexcept 

40  

41cdef extern from 'cuda_runtime_api.h' nogil: 

42 cudaError_t _static_cudaDeviceSetCacheConfig "cudaDeviceSetCacheConfig" (cudaFuncCache cacheConfig) noexcept 

43  

44cdef extern from 'cuda_runtime_api.h' nogil: 

45 cudaError_t _static_cudaDeviceGetByPCIBusId "cudaDeviceGetByPCIBusId" (int* device, const char* pciBusId) noexcept 

46  

47cdef extern from 'cuda_runtime_api.h' nogil: 

48 cudaError_t _static_cudaDeviceGetPCIBusId "cudaDeviceGetPCIBusId" (char* pciBusId, int len, int device) noexcept 

49  

50cdef extern from 'cuda_runtime_api.h' nogil: 

51 cudaError_t _static_cudaIpcGetEventHandle "cudaIpcGetEventHandle" (cudaIpcEventHandle_t* handle, cudaEvent_t event) noexcept 

52  

53cdef extern from 'cuda_runtime_api.h' nogil: 

54 cudaError_t _static_cudaIpcOpenEventHandle "cudaIpcOpenEventHandle" (cudaEvent_t* event, cudaIpcEventHandle_t handle) noexcept 

55  

56cdef extern from 'cuda_runtime_api.h' nogil: 

57 cudaError_t _static_cudaIpcGetMemHandle "cudaIpcGetMemHandle" (cudaIpcMemHandle_t* handle, void* devPtr) noexcept 

58  

59cdef extern from 'cuda_runtime_api.h' nogil: 

60 cudaError_t _static_cudaIpcOpenMemHandle "cudaIpcOpenMemHandle" (void** devPtr, cudaIpcMemHandle_t handle, unsigned int flags) noexcept 

61  

62cdef extern from 'cuda_runtime_api.h' nogil: 

63 cudaError_t _static_cudaIpcCloseMemHandle "cudaIpcCloseMemHandle" (void* devPtr) noexcept 

64  

65cdef extern from 'cuda_runtime_api.h' nogil: 

66 cudaError_t _static_cudaDeviceFlushGPUDirectRDMAWrites "cudaDeviceFlushGPUDirectRDMAWrites" (cudaFlushGPUDirectRDMAWritesTarget target, cudaFlushGPUDirectRDMAWritesScope scope) noexcept 

67  

68cdef extern from 'cuda_runtime_api.h' nogil: 

69 cudaError_t _static_cudaDeviceRegisterAsyncNotification "cudaDeviceRegisterAsyncNotification" (int device, cudaAsyncCallback callbackFunc, void* userData, cudaAsyncCallbackHandle_t* callback) noexcept 

70  

71cdef extern from 'cuda_runtime_api.h' nogil: 

72 cudaError_t _static_cudaDeviceUnregisterAsyncNotification "cudaDeviceUnregisterAsyncNotification" (int device, cudaAsyncCallbackHandle_t callback) noexcept 

73  

74cdef extern from 'cuda_runtime_api.h' nogil: 

75 cudaError_t _static_cudaDeviceGetSharedMemConfig "cudaDeviceGetSharedMemConfig" (cudaSharedMemConfig* pConfig) noexcept 

76  

77cdef extern from 'cuda_runtime_api.h' nogil: 

78 cudaError_t _static_cudaDeviceSetSharedMemConfig "cudaDeviceSetSharedMemConfig" (cudaSharedMemConfig config) noexcept 

79  

80cdef extern from 'cuda_runtime_api.h' nogil: 

81 cudaError_t _static_cudaGetLastError "cudaGetLastError" () noexcept 

82  

83cdef extern from 'cuda_runtime_api.h' nogil: 

84 cudaError_t _static_cudaPeekAtLastError "cudaPeekAtLastError" () noexcept 

85  

86cdef extern from 'cuda_runtime_api.h' nogil: 

87 const char* _static_cudaGetErrorName "cudaGetErrorName" (cudaError_t error) noexcept 

88  

89cdef extern from 'cuda_runtime_api.h' nogil: 

90 const char* _static_cudaGetErrorString "cudaGetErrorString" (cudaError_t error) noexcept 

91  

92cdef extern from 'cuda_runtime_api.h' nogil: 

93 cudaError_t _static_cudaGetDeviceCount "cudaGetDeviceCount" (int* count) noexcept 

94  

95cdef extern from 'cuda_runtime_api.h' nogil: 

96 cudaError_t _static_cudaDeviceGetAttribute "cudaDeviceGetAttribute" (int* value, cudaDeviceAttr attr, int device) noexcept 

97  

98cdef extern from 'cuda_runtime_api.h' nogil: 

99 cudaError_t _static_cudaDeviceGetDefaultMemPool "cudaDeviceGetDefaultMemPool" (cudaMemPool_t* memPool, int device) noexcept 

100  

101cdef extern from 'cuda_runtime_api.h' nogil: 

102 cudaError_t _static_cudaDeviceSetMemPool "cudaDeviceSetMemPool" (int device, cudaMemPool_t memPool) noexcept 

103  

104cdef extern from 'cuda_runtime_api.h' nogil: 

105 cudaError_t _static_cudaDeviceGetMemPool "cudaDeviceGetMemPool" (cudaMemPool_t* memPool, int device) noexcept 

106  

107cdef extern from 'cuda_runtime_api.h' nogil: 

108 cudaError_t _static_cudaDeviceGetNvSciSyncAttributes "cudaDeviceGetNvSciSyncAttributes" (void* nvSciSyncAttrList, int device, int flags) noexcept 

109  

110cdef extern from 'cuda_runtime_api.h' nogil: 

111 cudaError_t _static_cudaDeviceGetP2PAttribute "cudaDeviceGetP2PAttribute" (int* value, cudaDeviceP2PAttr attr, int srcDevice, int dstDevice) noexcept 

112  

113cdef extern from 'cuda_runtime_api.h' nogil: 

114 cudaError_t _static_cudaChooseDevice "cudaChooseDevice" (int* device, const cudaDeviceProp* prop) noexcept 

115  

116cdef extern from 'cuda_runtime_api.h' nogil: 

117 cudaError_t _static_cudaInitDevice "cudaInitDevice" (int device, unsigned int deviceFlags, unsigned int flags) noexcept 

118  

119cdef extern from 'cuda_runtime_api.h' nogil: 

120 cudaError_t _static_cudaSetDevice "cudaSetDevice" (int device) noexcept 

121  

122cdef extern from 'cuda_runtime_api.h' nogil: 

123 cudaError_t _static_cudaGetDevice "cudaGetDevice" (int* device) noexcept 

124  

125cdef extern from 'cuda_runtime_api.h' nogil: 

126 cudaError_t _static_cudaSetDeviceFlags "cudaSetDeviceFlags" (unsigned int flags) noexcept 

127  

128cdef extern from 'cuda_runtime_api.h' nogil: 

129 cudaError_t _static_cudaGetDeviceFlags "cudaGetDeviceFlags" (unsigned int* flags) noexcept 

130  

131cdef extern from 'cuda_runtime_api.h' nogil: 

132 cudaError_t _static_cudaStreamCreate "cudaStreamCreate" (cudaStream_t* pStream) noexcept 

133  

134cdef extern from 'cuda_runtime_api.h' nogil: 

135 cudaError_t _static_cudaStreamCreateWithFlags "cudaStreamCreateWithFlags" (cudaStream_t* pStream, unsigned int flags) noexcept 

136  

137cdef extern from 'cuda_runtime_api.h' nogil: 

138 cudaError_t _static_cudaStreamCreateWithPriority "cudaStreamCreateWithPriority" (cudaStream_t* pStream, unsigned int flags, int priority) noexcept 

139  

140cdef extern from 'cuda_runtime_api.h' nogil: 

141 cudaError_t _static_cudaStreamGetPriority "cudaStreamGetPriority" (cudaStream_t hStream, int* priority) noexcept 

142  

143cdef extern from 'cuda_runtime_api.h' nogil: 

144 cudaError_t _static_cudaStreamGetFlags "cudaStreamGetFlags" (cudaStream_t hStream, unsigned int* flags) noexcept 

145  

146cdef extern from 'cuda_runtime_api.h' nogil: 

147 cudaError_t _static_cudaStreamGetId "cudaStreamGetId" (cudaStream_t hStream, unsigned long long* streamId) noexcept 

148  

149cdef extern from 'cuda_runtime_api.h' nogil: 

150 cudaError_t _static_cudaStreamGetDevice "cudaStreamGetDevice" (cudaStream_t hStream, int* device) noexcept 

151  

152cdef extern from 'cuda_runtime_api.h' nogil: 

153 cudaError_t _static_cudaCtxResetPersistingL2Cache "cudaCtxResetPersistingL2Cache" () noexcept 

154  

155cdef extern from 'cuda_runtime_api.h' nogil: 

156 cudaError_t _static_cudaStreamCopyAttributes "cudaStreamCopyAttributes" (cudaStream_t dst, cudaStream_t src) noexcept 

157  

158cdef extern from 'cuda_runtime_api.h' nogil: 

159 cudaError_t _static_cudaStreamGetAttribute "cudaStreamGetAttribute" (cudaStream_t hStream, cudaLaunchAttributeID attr, cudaLaunchAttributeValue* value_out) noexcept 

160  

161cdef extern from 'cuda_runtime_api.h' nogil: 

162 cudaError_t _static_cudaStreamSetAttribute "cudaStreamSetAttribute" (cudaStream_t hStream, cudaLaunchAttributeID attr, const cudaLaunchAttributeValue* value) noexcept 

163  

164cdef extern from 'cuda_runtime_api.h' nogil: 

165 cudaError_t _static_cudaStreamDestroy "cudaStreamDestroy" (cudaStream_t stream) noexcept 

166  

167cdef extern from 'cuda_runtime_api.h' nogil: 

168 cudaError_t _static_cudaStreamWaitEvent "cudaStreamWaitEvent" (cudaStream_t stream, cudaEvent_t event, unsigned int flags) noexcept 

169  

170cdef extern from 'cuda_runtime_api.h' nogil: 

171 cudaError_t _static_cudaStreamAddCallback "cudaStreamAddCallback" (cudaStream_t stream, cudaStreamCallback_t callback, void* userData, unsigned int flags) noexcept 

172  

173cdef extern from 'cuda_runtime_api.h' nogil: 

174 cudaError_t _static_cudaStreamSynchronize "cudaStreamSynchronize" (cudaStream_t stream) noexcept 

175  

176cdef extern from 'cuda_runtime_api.h' nogil: 

177 cudaError_t _static_cudaStreamQuery "cudaStreamQuery" (cudaStream_t stream) noexcept 

178  

179cdef extern from 'cuda_runtime_api.h' nogil: 

180 cudaError_t _static_cudaStreamAttachMemAsync "cudaStreamAttachMemAsync" (cudaStream_t stream, void* devPtr, size_t length, unsigned int flags) noexcept 

181  

182cdef extern from 'cuda_runtime_api.h' nogil: 

183 cudaError_t _static_cudaStreamBeginCapture "cudaStreamBeginCapture" (cudaStream_t stream, cudaStreamCaptureMode mode) noexcept 

184  

185cdef extern from 'cuda_runtime_api.h' nogil: 

186 cudaError_t _static_cudaStreamBeginCaptureToGraph "cudaStreamBeginCaptureToGraph" (cudaStream_t stream, cudaGraph_t graph, const cudaGraphNode_t* dependencies, const cudaGraphEdgeData* dependencyData, size_t numDependencies, cudaStreamCaptureMode mode) noexcept 

187  

188cdef extern from 'cuda_runtime_api.h' nogil: 

189 cudaError_t _static_cudaThreadExchangeStreamCaptureMode "cudaThreadExchangeStreamCaptureMode" (cudaStreamCaptureMode* mode) noexcept 

190  

191cdef extern from 'cuda_runtime_api.h' nogil: 

192 cudaError_t _static_cudaStreamEndCapture "cudaStreamEndCapture" (cudaStream_t stream, cudaGraph_t* pGraph) noexcept 

193  

194cdef extern from 'cuda_runtime_api.h' nogil: 

195 cudaError_t _static_cudaStreamIsCapturing "cudaStreamIsCapturing" (cudaStream_t stream, cudaStreamCaptureStatus* pCaptureStatus) noexcept 

196  

197cdef extern from 'cuda_runtime_api.h' nogil: 

198 cudaError_t _static_cudaStreamUpdateCaptureDependencies "cudaStreamUpdateCaptureDependencies" (cudaStream_t stream, cudaGraphNode_t* dependencies, const cudaGraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) noexcept 

199  

200cdef extern from 'cuda_runtime_api.h' nogil: 

201 cudaError_t _static_cudaEventCreate "cudaEventCreate" (cudaEvent_t* event) noexcept 

202  

203cdef extern from 'cuda_runtime_api.h' nogil: 

204 cudaError_t _static_cudaEventCreateWithFlags "cudaEventCreateWithFlags" (cudaEvent_t* event, unsigned int flags) noexcept 

205  

206cdef extern from 'cuda_runtime_api.h' nogil: 

207 cudaError_t _static_cudaEventRecord "cudaEventRecord" (cudaEvent_t event, cudaStream_t stream) noexcept 

208  

209cdef extern from 'cuda_runtime_api.h' nogil: 

210 cudaError_t _static_cudaEventRecordWithFlags "cudaEventRecordWithFlags" (cudaEvent_t event, cudaStream_t stream, unsigned int flags) noexcept 

211  

212cdef extern from 'cuda_runtime_api.h' nogil: 

213 cudaError_t _static_cudaEventQuery "cudaEventQuery" (cudaEvent_t event) noexcept 

214  

215cdef extern from 'cuda_runtime_api.h' nogil: 

216 cudaError_t _static_cudaEventSynchronize "cudaEventSynchronize" (cudaEvent_t event) noexcept 

217  

218cdef extern from 'cuda_runtime_api.h' nogil: 

219 cudaError_t _static_cudaEventDestroy "cudaEventDestroy" (cudaEvent_t event) noexcept 

220  

221cdef extern from 'cuda_runtime_api.h' nogil: 

222 cudaError_t _static_cudaEventElapsedTime "cudaEventElapsedTime" (float* ms, cudaEvent_t start, cudaEvent_t end) noexcept 

223  

224cdef extern from 'cuda_runtime_api.h' nogil: 

225 cudaError_t _static_cudaImportExternalMemory "cudaImportExternalMemory" (cudaExternalMemory_t* extMem_out, const cudaExternalMemoryHandleDesc* memHandleDesc) noexcept 

226  

227cdef extern from 'cuda_runtime_api.h' nogil: 

228 cudaError_t _static_cudaExternalMemoryGetMappedBuffer "cudaExternalMemoryGetMappedBuffer" (void** devPtr, cudaExternalMemory_t extMem, const cudaExternalMemoryBufferDesc* bufferDesc) noexcept 

229  

230cdef extern from 'cuda_runtime_api.h' nogil: 

231 cudaError_t _static_cudaExternalMemoryGetMappedMipmappedArray "cudaExternalMemoryGetMappedMipmappedArray" (cudaMipmappedArray_t* mipmap, cudaExternalMemory_t extMem, const cudaExternalMemoryMipmappedArrayDesc* mipmapDesc) noexcept 

232  

233cdef extern from 'cuda_runtime_api.h' nogil: 

234 cudaError_t _static_cudaDestroyExternalMemory "cudaDestroyExternalMemory" (cudaExternalMemory_t extMem) noexcept 

235  

236cdef extern from 'cuda_runtime_api.h' nogil: 

237 cudaError_t _static_cudaImportExternalSemaphore "cudaImportExternalSemaphore" (cudaExternalSemaphore_t* extSem_out, const cudaExternalSemaphoreHandleDesc* semHandleDesc) noexcept 

238  

239cdef extern from 'cuda_runtime_api.h' nogil: 

240 cudaError_t _static_cudaDestroyExternalSemaphore "cudaDestroyExternalSemaphore" (cudaExternalSemaphore_t extSem) noexcept 

241  

242cdef extern from 'cuda_runtime_api.h' nogil: 

243 cudaError_t _static_cudaFuncSetCacheConfig "cudaFuncSetCacheConfig" (const void* func, cudaFuncCache cacheConfig) noexcept 

244  

245cdef extern from 'cuda_runtime_api.h' nogil: 

246 cudaError_t _static_cudaFuncGetAttributes "cudaFuncGetAttributes" (cudaFuncAttributes* attr, const void* func) noexcept 

247  

248cdef extern from 'cuda_runtime_api.h' nogil: 

249 cudaError_t _static_cudaFuncSetAttribute "cudaFuncSetAttribute" (const void* func, cudaFuncAttribute attr, int value) noexcept 

250  

251cdef extern from 'cuda_runtime_api.h' nogil: 

252 cudaError_t _static_cudaFuncGetName "cudaFuncGetName" (const char** name, const void* func) noexcept 

253  

254cdef extern from 'cuda_runtime_api.h' nogil: 

255 cudaError_t _static_cudaFuncGetParamInfo "cudaFuncGetParamInfo" (const void* func, size_t paramIndex, size_t* paramOffset, size_t* paramSize) noexcept 

256  

257cdef extern from 'cuda_runtime_api.h' nogil: 

258 cudaError_t _static_cudaLaunchHostFunc "cudaLaunchHostFunc" (cudaStream_t stream, cudaHostFn_t fn, void* userData) noexcept 

259  

260cdef extern from 'cuda_runtime_api.h' nogil: 

261 cudaError_t _static_cudaFuncSetSharedMemConfig "cudaFuncSetSharedMemConfig" (const void* func, cudaSharedMemConfig config) noexcept 

262  

263cdef extern from 'cuda_runtime_api.h' nogil: 

264 cudaError_t _static_cudaOccupancyMaxActiveBlocksPerMultiprocessor "cudaOccupancyMaxActiveBlocksPerMultiprocessor" (int* numBlocks, const void* func, int blockSize, size_t dynamicSMemSize) noexcept 

265  

266cdef extern from 'cuda_runtime_api.h' nogil: 

267 cudaError_t _static_cudaOccupancyAvailableDynamicSMemPerBlock "cudaOccupancyAvailableDynamicSMemPerBlock" (size_t* dynamicSmemSize, const void* func, int numBlocks, int blockSize) noexcept 

268  

269cdef extern from 'cuda_runtime_api.h' nogil: 

270 cudaError_t _static_cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags "cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags" (int* numBlocks, const void* func, int blockSize, size_t dynamicSMemSize, unsigned int flags) noexcept 

271  

272cdef extern from 'cuda_runtime_api.h' nogil: 

273 cudaError_t _static_cudaMallocManaged "cudaMallocManaged" (void** devPtr, size_t size, unsigned int flags) noexcept 

274  

275cdef extern from 'cuda_runtime_api.h' nogil: 

276 cudaError_t _static_cudaMalloc "cudaMalloc" (void** devPtr, size_t size) noexcept 

277  

278cdef extern from 'cuda_runtime_api.h' nogil: 

279 cudaError_t _static_cudaMallocHost "cudaMallocHost" (void** ptr, size_t size) noexcept 

280  

281cdef extern from 'cuda_runtime_api.h' nogil: 

282 cudaError_t _static_cudaMallocPitch "cudaMallocPitch" (void** devPtr, size_t* pitch, size_t width, size_t height) noexcept 

283  

284cdef extern from 'cuda_runtime_api.h' nogil: 

285 cudaError_t _static_cudaMallocArray "cudaMallocArray" (cudaArray_t* array, const cudaChannelFormatDesc* desc, size_t width, size_t height, unsigned int flags) noexcept 

286  

287cdef extern from 'cuda_runtime_api.h' nogil: 

288 cudaError_t _static_cudaFree "cudaFree" (void* devPtr) noexcept 

289  

290cdef extern from 'cuda_runtime_api.h' nogil: 

291 cudaError_t _static_cudaFreeHost "cudaFreeHost" (void* ptr) noexcept 

292  

293cdef extern from 'cuda_runtime_api.h' nogil: 

294 cudaError_t _static_cudaFreeArray "cudaFreeArray" (cudaArray_t array) noexcept 

295  

296cdef extern from 'cuda_runtime_api.h' nogil: 

297 cudaError_t _static_cudaFreeMipmappedArray "cudaFreeMipmappedArray" (cudaMipmappedArray_t mipmappedArray) noexcept 

298  

299cdef extern from 'cuda_runtime_api.h' nogil: 

300 cudaError_t _static_cudaHostAlloc "cudaHostAlloc" (void** pHost, size_t size, unsigned int flags) noexcept 

301  

302cdef extern from 'cuda_runtime_api.h' nogil: 

303 cudaError_t _static_cudaHostRegister "cudaHostRegister" (void* ptr, size_t size, unsigned int flags) noexcept 

304  

305cdef extern from 'cuda_runtime_api.h' nogil: 

306 cudaError_t _static_cudaHostUnregister "cudaHostUnregister" (void* ptr) noexcept 

307  

308cdef extern from 'cuda_runtime_api.h' nogil: 

309 cudaError_t _static_cudaHostGetDevicePointer "cudaHostGetDevicePointer" (void** pDevice, void* pHost, unsigned int flags) noexcept 

310  

311cdef extern from 'cuda_runtime_api.h' nogil: 

312 cudaError_t _static_cudaHostGetFlags "cudaHostGetFlags" (unsigned int* pFlags, void* pHost) noexcept 

313  

314cdef extern from 'cuda_runtime_api.h' nogil: 

315 cudaError_t _static_cudaMalloc3D "cudaMalloc3D" (cudaPitchedPtr* pitchedDevPtr, cudaExtent extent) noexcept 

316  

317cdef extern from 'cuda_runtime_api.h' nogil: 

318 cudaError_t _static_cudaMalloc3DArray "cudaMalloc3DArray" (cudaArray_t* array, const cudaChannelFormatDesc* desc, cudaExtent extent, unsigned int flags) noexcept 

319  

320cdef extern from 'cuda_runtime_api.h' nogil: 

321 cudaError_t _static_cudaMallocMipmappedArray "cudaMallocMipmappedArray" (cudaMipmappedArray_t* mipmappedArray, const cudaChannelFormatDesc* desc, cudaExtent extent, unsigned int numLevels, unsigned int flags) noexcept 

322  

323cdef extern from 'cuda_runtime_api.h' nogil: 

324 cudaError_t _static_cudaGetMipmappedArrayLevel "cudaGetMipmappedArrayLevel" (cudaArray_t* levelArray, cudaMipmappedArray_const_t mipmappedArray, unsigned int level) noexcept 

325  

326cdef extern from 'cuda_runtime_api.h' nogil: 

327 cudaError_t _static_cudaMemcpy3D "cudaMemcpy3D" (const cudaMemcpy3DParms* p) noexcept 

328  

329cdef extern from 'cuda_runtime_api.h' nogil: 

330 cudaError_t _static_cudaMemcpy3DPeer "cudaMemcpy3DPeer" (const cudaMemcpy3DPeerParms* p) noexcept 

331  

332cdef extern from 'cuda_runtime_api.h' nogil: 

333 cudaError_t _static_cudaMemcpy3DAsync "cudaMemcpy3DAsync" (const cudaMemcpy3DParms* p, cudaStream_t stream) noexcept 

334  

335cdef extern from 'cuda_runtime_api.h' nogil: 

336 cudaError_t _static_cudaMemcpy3DPeerAsync "cudaMemcpy3DPeerAsync" (const cudaMemcpy3DPeerParms* p, cudaStream_t stream) noexcept 

337  

338cdef extern from 'cuda_runtime_api.h' nogil: 

339 cudaError_t _static_cudaMemGetInfo "cudaMemGetInfo" (size_t* free, size_t* total) noexcept 

340  

341cdef extern from 'cuda_runtime_api.h' nogil: 

342 cudaError_t _static_cudaArrayGetInfo "cudaArrayGetInfo" (cudaChannelFormatDesc* desc, cudaExtent* extent, unsigned int* flags, cudaArray_t array) noexcept 

343  

344cdef extern from 'cuda_runtime_api.h' nogil: 

345 cudaError_t _static_cudaArrayGetPlane "cudaArrayGetPlane" (cudaArray_t* pPlaneArray, cudaArray_t hArray, unsigned int planeIdx) noexcept 

346  

347cdef extern from 'cuda_runtime_api.h' nogil: 

348 cudaError_t _static_cudaArrayGetMemoryRequirements "cudaArrayGetMemoryRequirements" (cudaArrayMemoryRequirements* memoryRequirements, cudaArray_t array, int device) noexcept 

349  

350cdef extern from 'cuda_runtime_api.h' nogil: 

351 cudaError_t _static_cudaMipmappedArrayGetMemoryRequirements "cudaMipmappedArrayGetMemoryRequirements" (cudaArrayMemoryRequirements* memoryRequirements, cudaMipmappedArray_t mipmap, int device) noexcept 

352  

353cdef extern from 'cuda_runtime_api.h' nogil: 

354 cudaError_t _static_cudaArrayGetSparseProperties "cudaArrayGetSparseProperties" (cudaArraySparseProperties* sparseProperties, cudaArray_t array) noexcept 

355  

356cdef extern from 'cuda_runtime_api.h' nogil: 

357 cudaError_t _static_cudaMipmappedArrayGetSparseProperties "cudaMipmappedArrayGetSparseProperties" (cudaArraySparseProperties* sparseProperties, cudaMipmappedArray_t mipmap) noexcept 

358  

359cdef extern from 'cuda_runtime_api.h' nogil: 

360 cudaError_t _static_cudaMemcpy "cudaMemcpy" (void* dst, const void* src, size_t count, cudaMemcpyKind kind) noexcept 

361  

362cdef extern from 'cuda_runtime_api.h' nogil: 

363 cudaError_t _static_cudaMemcpyPeer "cudaMemcpyPeer" (void* dst, int dstDevice, const void* src, int srcDevice, size_t count) noexcept 

364  

365cdef extern from 'cuda_runtime_api.h' nogil: 

366 cudaError_t _static_cudaMemcpy2D "cudaMemcpy2D" (void* dst, size_t dpitch, const void* src, size_t spitch, size_t width, size_t height, cudaMemcpyKind kind) noexcept 

367  

368cdef extern from 'cuda_runtime_api.h' nogil: 

369 cudaError_t _static_cudaMemcpy2DToArray "cudaMemcpy2DToArray" (cudaArray_t dst, size_t wOffset, size_t hOffset, const void* src, size_t spitch, size_t width, size_t height, cudaMemcpyKind kind) noexcept 

370  

371cdef extern from 'cuda_runtime_api.h' nogil: 

372 cudaError_t _static_cudaMemcpy2DFromArray "cudaMemcpy2DFromArray" (void* dst, size_t dpitch, cudaArray_const_t src, size_t wOffset, size_t hOffset, size_t width, size_t height, cudaMemcpyKind kind) noexcept 

373  

374cdef extern from 'cuda_runtime_api.h' nogil: 

375 cudaError_t _static_cudaMemcpy2DArrayToArray "cudaMemcpy2DArrayToArray" (cudaArray_t dst, size_t wOffsetDst, size_t hOffsetDst, cudaArray_const_t src, size_t wOffsetSrc, size_t hOffsetSrc, size_t width, size_t height, cudaMemcpyKind kind) noexcept 

376  

377cdef extern from 'cuda_runtime_api.h' nogil: 

378 cudaError_t _static_cudaMemcpyAsync "cudaMemcpyAsync" (void* dst, const void* src, size_t count, cudaMemcpyKind kind, cudaStream_t stream) noexcept 

379  

380cdef extern from 'cuda_runtime_api.h' nogil: 

381 cudaError_t _static_cudaMemcpyPeerAsync "cudaMemcpyPeerAsync" (void* dst, int dstDevice, const void* src, int srcDevice, size_t count, cudaStream_t stream) noexcept 

382  

383cdef extern from 'cuda_runtime_api.h' nogil: 

384 cudaError_t _static_cudaMemcpyBatchAsync "cudaMemcpyBatchAsync" (void** dsts, const void** srcs, const size_t* sizes, size_t count, cudaMemcpyAttributes* attrs, size_t* attrsIdxs, size_t numAttrs, cudaStream_t stream) noexcept 

385  

386cdef extern from 'cuda_runtime_api.h' nogil: 

387 cudaError_t _static_cudaMemcpy3DBatchAsync "cudaMemcpy3DBatchAsync" (size_t numOps, cudaMemcpy3DBatchOp* opList, unsigned long long flags, cudaStream_t stream) noexcept 

388  

389cdef extern from 'cuda_runtime_api.h' nogil: 

390 cudaError_t _static_cudaMemcpy2DAsync "cudaMemcpy2DAsync" (void* dst, size_t dpitch, const void* src, size_t spitch, size_t width, size_t height, cudaMemcpyKind kind, cudaStream_t stream) noexcept 

391  

392cdef extern from 'cuda_runtime_api.h' nogil: 

393 cudaError_t _static_cudaMemcpy2DToArrayAsync "cudaMemcpy2DToArrayAsync" (cudaArray_t dst, size_t wOffset, size_t hOffset, const void* src, size_t spitch, size_t width, size_t height, cudaMemcpyKind kind, cudaStream_t stream) noexcept 

394  

395cdef extern from 'cuda_runtime_api.h' nogil: 

396 cudaError_t _static_cudaMemcpy2DFromArrayAsync "cudaMemcpy2DFromArrayAsync" (void* dst, size_t dpitch, cudaArray_const_t src, size_t wOffset, size_t hOffset, size_t width, size_t height, cudaMemcpyKind kind, cudaStream_t stream) noexcept 

397  

398cdef extern from 'cuda_runtime_api.h' nogil: 

399 cudaError_t _static_cudaMemset "cudaMemset" (void* devPtr, int value, size_t count) noexcept 

400  

401cdef extern from 'cuda_runtime_api.h' nogil: 

402 cudaError_t _static_cudaMemset2D "cudaMemset2D" (void* devPtr, size_t pitch, int value, size_t width, size_t height) noexcept 

403  

404cdef extern from 'cuda_runtime_api.h' nogil: 

405 cudaError_t _static_cudaMemset3D "cudaMemset3D" (cudaPitchedPtr pitchedDevPtr, int value, cudaExtent extent) noexcept 

406  

407cdef extern from 'cuda_runtime_api.h' nogil: 

408 cudaError_t _static_cudaMemsetAsync "cudaMemsetAsync" (void* devPtr, int value, size_t count, cudaStream_t stream) noexcept 

409  

410cdef extern from 'cuda_runtime_api.h' nogil: 

411 cudaError_t _static_cudaMemset2DAsync "cudaMemset2DAsync" (void* devPtr, size_t pitch, int value, size_t width, size_t height, cudaStream_t stream) noexcept 

412  

413cdef extern from 'cuda_runtime_api.h' nogil: 

414 cudaError_t _static_cudaMemset3DAsync "cudaMemset3DAsync" (cudaPitchedPtr pitchedDevPtr, int value, cudaExtent extent, cudaStream_t stream) noexcept 

415  

416cdef extern from 'cuda_runtime_api.h' nogil: 

417 cudaError_t _static_cudaMemPrefetchAsync "cudaMemPrefetchAsync" (const void* devPtr, size_t count, cudaMemLocation location, unsigned int flags, cudaStream_t stream) noexcept 

418  

419cdef extern from 'cuda_runtime_api.h' nogil: 

420 cudaError_t _static_cudaMemAdvise "cudaMemAdvise" (const void* devPtr, size_t count, cudaMemoryAdvise advice, cudaMemLocation location) noexcept 

421  

422cdef extern from 'cuda_runtime_api.h' nogil: 

423 cudaError_t _static_cudaMemRangeGetAttribute "cudaMemRangeGetAttribute" (void* data, size_t dataSize, cudaMemRangeAttribute attribute, const void* devPtr, size_t count) noexcept 

424  

425cdef extern from 'cuda_runtime_api.h' nogil: 

426 cudaError_t _static_cudaMemRangeGetAttributes "cudaMemRangeGetAttributes" (void** data, size_t* dataSizes, cudaMemRangeAttribute* attributes, size_t numAttributes, const void* devPtr, size_t count) noexcept 

427  

428cdef extern from 'cuda_runtime_api.h' nogil: 

429 cudaError_t _static_cudaMemcpyToArray "cudaMemcpyToArray" (cudaArray_t dst, size_t wOffset, size_t hOffset, const void* src, size_t count, cudaMemcpyKind kind) noexcept 

430  

431cdef extern from 'cuda_runtime_api.h' nogil: 

432 cudaError_t _static_cudaMemcpyFromArray "cudaMemcpyFromArray" (void* dst, cudaArray_const_t src, size_t wOffset, size_t hOffset, size_t count, cudaMemcpyKind kind) noexcept 

433  

434cdef extern from 'cuda_runtime_api.h' nogil: 

435 cudaError_t _static_cudaMemcpyArrayToArray "cudaMemcpyArrayToArray" (cudaArray_t dst, size_t wOffsetDst, size_t hOffsetDst, cudaArray_const_t src, size_t wOffsetSrc, size_t hOffsetSrc, size_t count, cudaMemcpyKind kind) noexcept 

436  

437cdef extern from 'cuda_runtime_api.h' nogil: 

438 cudaError_t _static_cudaMemcpyToArrayAsync "cudaMemcpyToArrayAsync" (cudaArray_t dst, size_t wOffset, size_t hOffset, const void* src, size_t count, cudaMemcpyKind kind, cudaStream_t stream) noexcept 

439  

440cdef extern from 'cuda_runtime_api.h' nogil: 

441 cudaError_t _static_cudaMemcpyFromArrayAsync "cudaMemcpyFromArrayAsync" (void* dst, cudaArray_const_t src, size_t wOffset, size_t hOffset, size_t count, cudaMemcpyKind kind, cudaStream_t stream) noexcept 

442  

443cdef extern from 'cuda_runtime_api.h' nogil: 

444 cudaError_t _static_cudaMallocAsync "cudaMallocAsync" (void** devPtr, size_t size, cudaStream_t hStream) noexcept 

445  

446cdef extern from 'cuda_runtime_api.h' nogil: 

447 cudaError_t _static_cudaFreeAsync "cudaFreeAsync" (void* devPtr, cudaStream_t hStream) noexcept 

448  

449cdef extern from 'cuda_runtime_api.h' nogil: 

450 cudaError_t _static_cudaMemPoolTrimTo "cudaMemPoolTrimTo" (cudaMemPool_t memPool, size_t minBytesToKeep) noexcept 

451  

452cdef extern from 'cuda_runtime_api.h' nogil: 

453 cudaError_t _static_cudaMemPoolSetAttribute "cudaMemPoolSetAttribute" (cudaMemPool_t memPool, cudaMemPoolAttr attr, void* value) noexcept 

454  

455cdef extern from 'cuda_runtime_api.h' nogil: 

456 cudaError_t _static_cudaMemPoolGetAttribute "cudaMemPoolGetAttribute" (cudaMemPool_t memPool, cudaMemPoolAttr attr, void* value) noexcept 

457  

458cdef extern from 'cuda_runtime_api.h' nogil: 

459 cudaError_t _static_cudaMemPoolSetAccess "cudaMemPoolSetAccess" (cudaMemPool_t memPool, const cudaMemAccessDesc* descList, size_t count) noexcept 

460  

461cdef extern from 'cuda_runtime_api.h' nogil: 

462 cudaError_t _static_cudaMemPoolGetAccess "cudaMemPoolGetAccess" (cudaMemAccessFlags* flags, cudaMemPool_t memPool, cudaMemLocation* location) noexcept 

463  

464cdef extern from 'cuda_runtime_api.h' nogil: 

465 cudaError_t _static_cudaMemPoolCreate "cudaMemPoolCreate" (cudaMemPool_t* memPool, const cudaMemPoolProps* poolProps) noexcept 

466  

467cdef extern from 'cuda_runtime_api.h' nogil: 

468 cudaError_t _static_cudaMemPoolDestroy "cudaMemPoolDestroy" (cudaMemPool_t memPool) noexcept 

469  

470cdef extern from 'cuda_runtime_api.h' nogil: 

471 cudaError_t _static_cudaMallocFromPoolAsync "cudaMallocFromPoolAsync" (void** ptr, size_t size, cudaMemPool_t memPool, cudaStream_t stream) noexcept 

472  

473cdef extern from 'cuda_runtime_api.h' nogil: 

474 cudaError_t _static_cudaMemPoolExportToShareableHandle "cudaMemPoolExportToShareableHandle" (void* shareableHandle, cudaMemPool_t memPool, cudaMemAllocationHandleType handleType, unsigned int flags) noexcept 

475  

476cdef extern from 'cuda_runtime_api.h' nogil: 

477 cudaError_t _static_cudaMemPoolImportFromShareableHandle "cudaMemPoolImportFromShareableHandle" (cudaMemPool_t* memPool, void* shareableHandle, cudaMemAllocationHandleType handleType, unsigned int flags) noexcept 

478  

479cdef extern from 'cuda_runtime_api.h' nogil: 

480 cudaError_t _static_cudaMemPoolExportPointer "cudaMemPoolExportPointer" (cudaMemPoolPtrExportData* exportData, void* ptr) noexcept 

481  

482cdef extern from 'cuda_runtime_api.h' nogil: 

483 cudaError_t _static_cudaMemPoolImportPointer "cudaMemPoolImportPointer" (void** ptr, cudaMemPool_t memPool, cudaMemPoolPtrExportData* exportData) noexcept 

484  

485cdef extern from 'cuda_runtime_api.h' nogil: 

486 cudaError_t _static_cudaPointerGetAttributes "cudaPointerGetAttributes" (cudaPointerAttributes* attributes, const void* ptr) noexcept 

487  

488cdef extern from 'cuda_runtime_api.h' nogil: 

489 cudaError_t _static_cudaDeviceCanAccessPeer "cudaDeviceCanAccessPeer" (int* canAccessPeer, int device, int peerDevice) noexcept 

490  

491cdef extern from 'cuda_runtime_api.h' nogil: 

492 cudaError_t _static_cudaDeviceEnablePeerAccess "cudaDeviceEnablePeerAccess" (int peerDevice, unsigned int flags) noexcept 

493  

494cdef extern from 'cuda_runtime_api.h' nogil: 

495 cudaError_t _static_cudaDeviceDisablePeerAccess "cudaDeviceDisablePeerAccess" (int peerDevice) noexcept 

496  

497cdef extern from 'cuda_runtime_api.h' nogil: 

498 cudaError_t _static_cudaGraphicsUnregisterResource "cudaGraphicsUnregisterResource" (cudaGraphicsResource_t resource) noexcept 

499  

500cdef extern from 'cuda_runtime_api.h' nogil: 

501 cudaError_t _static_cudaGraphicsResourceSetMapFlags "cudaGraphicsResourceSetMapFlags" (cudaGraphicsResource_t resource, unsigned int flags) noexcept 

502  

503cdef extern from 'cuda_runtime_api.h' nogil: 

504 cudaError_t _static_cudaGraphicsMapResources "cudaGraphicsMapResources" (int count, cudaGraphicsResource_t* resources, cudaStream_t stream) noexcept 

505  

506cdef extern from 'cuda_runtime_api.h' nogil: 

507 cudaError_t _static_cudaGraphicsUnmapResources "cudaGraphicsUnmapResources" (int count, cudaGraphicsResource_t* resources, cudaStream_t stream) noexcept 

508  

509cdef extern from 'cuda_runtime_api.h' nogil: 

510 cudaError_t _static_cudaGraphicsResourceGetMappedPointer "cudaGraphicsResourceGetMappedPointer" (void** devPtr, size_t* size, cudaGraphicsResource_t resource) noexcept 

511  

512cdef extern from 'cuda_runtime_api.h' nogil: 

513 cudaError_t _static_cudaGraphicsSubResourceGetMappedArray "cudaGraphicsSubResourceGetMappedArray" (cudaArray_t* array, cudaGraphicsResource_t resource, unsigned int arrayIndex, unsigned int mipLevel) noexcept 

514  

515cdef extern from 'cuda_runtime_api.h' nogil: 

516 cudaError_t _static_cudaGraphicsResourceGetMappedMipmappedArray "cudaGraphicsResourceGetMappedMipmappedArray" (cudaMipmappedArray_t* mipmappedArray, cudaGraphicsResource_t resource) noexcept 

517  

518cdef extern from 'cuda_runtime_api.h' nogil: 

519 cudaError_t _static_cudaGetChannelDesc "cudaGetChannelDesc" (cudaChannelFormatDesc* desc, cudaArray_const_t array) noexcept 

520  

521cdef extern from 'cuda_runtime_api.h' nogil: 

522 cudaChannelFormatDesc _static_cudaCreateChannelDesc "cudaCreateChannelDesc" (int x, int y, int z, int w, cudaChannelFormatKind f) noexcept 

523  

524cdef extern from 'cuda_runtime_api.h' nogil: 

525 cudaError_t _static_cudaCreateTextureObject "cudaCreateTextureObject" (cudaTextureObject_t* pTexObject, const cudaResourceDesc* pResDesc, const cudaTextureDesc* pTexDesc, const cudaResourceViewDesc* pResViewDesc) noexcept 

526  

527cdef extern from 'cuda_runtime_api.h' nogil: 

528 cudaError_t _static_cudaDestroyTextureObject "cudaDestroyTextureObject" (cudaTextureObject_t texObject) noexcept 

529  

530cdef extern from 'cuda_runtime_api.h' nogil: 

531 cudaError_t _static_cudaGetTextureObjectResourceDesc "cudaGetTextureObjectResourceDesc" (cudaResourceDesc* pResDesc, cudaTextureObject_t texObject) noexcept 

532  

533cdef extern from 'cuda_runtime_api.h' nogil: 

534 cudaError_t _static_cudaGetTextureObjectTextureDesc "cudaGetTextureObjectTextureDesc" (cudaTextureDesc* pTexDesc, cudaTextureObject_t texObject) noexcept 

535  

536cdef extern from 'cuda_runtime_api.h' nogil: 

537 cudaError_t _static_cudaGetTextureObjectResourceViewDesc "cudaGetTextureObjectResourceViewDesc" (cudaResourceViewDesc* pResViewDesc, cudaTextureObject_t texObject) noexcept 

538  

539cdef extern from 'cuda_runtime_api.h' nogil: 

540 cudaError_t _static_cudaCreateSurfaceObject "cudaCreateSurfaceObject" (cudaSurfaceObject_t* pSurfObject, const cudaResourceDesc* pResDesc) noexcept 

541  

542cdef extern from 'cuda_runtime_api.h' nogil: 

543 cudaError_t _static_cudaDestroySurfaceObject "cudaDestroySurfaceObject" (cudaSurfaceObject_t surfObject) noexcept 

544  

545cdef extern from 'cuda_runtime_api.h' nogil: 

546 cudaError_t _static_cudaGetSurfaceObjectResourceDesc "cudaGetSurfaceObjectResourceDesc" (cudaResourceDesc* pResDesc, cudaSurfaceObject_t surfObject) noexcept 

547  

548cdef extern from 'cuda_runtime_api.h' nogil: 

549 cudaError_t _static_cudaDriverGetVersion "cudaDriverGetVersion" (int* driverVersion) noexcept 

550  

551cdef extern from 'cuda_runtime_api.h' nogil: 

552 cudaError_t _static_cudaRuntimeGetVersion "cudaRuntimeGetVersion" (int* runtimeVersion) noexcept 

553  

554cdef extern from 'cuda_runtime_api.h' nogil: 

555 cudaError_t _static_cudaGraphCreate "cudaGraphCreate" (cudaGraph_t* pGraph, unsigned int flags) noexcept 

556  

557cdef extern from 'cuda_runtime_api.h' nogil: 

558 cudaError_t _static_cudaGraphAddKernelNode "cudaGraphAddKernelNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaKernelNodeParams* pNodeParams) noexcept 

559  

560cdef extern from 'cuda_runtime_api.h' nogil: 

561 cudaError_t _static_cudaGraphKernelNodeGetParams "cudaGraphKernelNodeGetParams" (cudaGraphNode_t node, cudaKernelNodeParams* pNodeParams) noexcept 

562  

563cdef extern from 'cuda_runtime_api.h' nogil: 

564 cudaError_t _static_cudaGraphKernelNodeSetParams "cudaGraphKernelNodeSetParams" (cudaGraphNode_t node, const cudaKernelNodeParams* pNodeParams) noexcept 

565  

566cdef extern from 'cuda_runtime_api.h' nogil: 

567 cudaError_t _static_cudaGraphKernelNodeCopyAttributes "cudaGraphKernelNodeCopyAttributes" (cudaGraphNode_t hDst, cudaGraphNode_t hSrc) noexcept 

568  

569cdef extern from 'cuda_runtime_api.h' nogil: 

570 cudaError_t _static_cudaGraphKernelNodeGetAttribute "cudaGraphKernelNodeGetAttribute" (cudaGraphNode_t hNode, cudaLaunchAttributeID attr, cudaLaunchAttributeValue* value_out) noexcept 

571  

572cdef extern from 'cuda_runtime_api.h' nogil: 

573 cudaError_t _static_cudaGraphKernelNodeSetAttribute "cudaGraphKernelNodeSetAttribute" (cudaGraphNode_t hNode, cudaLaunchAttributeID attr, const cudaLaunchAttributeValue* value) noexcept 

574  

575cdef extern from 'cuda_runtime_api.h' nogil: 

576 cudaError_t _static_cudaGraphAddMemcpyNode "cudaGraphAddMemcpyNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaMemcpy3DParms* pCopyParams) noexcept 

577  

578cdef extern from 'cuda_runtime_api.h' nogil: 

579 cudaError_t _static_cudaGraphAddMemcpyNode1D "cudaGraphAddMemcpyNode1D" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, void* dst, const void* src, size_t count, cudaMemcpyKind kind) noexcept 

580  

581cdef extern from 'cuda_runtime_api.h' nogil: 

582 cudaError_t _static_cudaGraphMemcpyNodeGetParams "cudaGraphMemcpyNodeGetParams" (cudaGraphNode_t node, cudaMemcpy3DParms* pNodeParams) noexcept 

583  

584cdef extern from 'cuda_runtime_api.h' nogil: 

585 cudaError_t _static_cudaGraphMemcpyNodeSetParams "cudaGraphMemcpyNodeSetParams" (cudaGraphNode_t node, const cudaMemcpy3DParms* pNodeParams) noexcept 

586  

587cdef extern from 'cuda_runtime_api.h' nogil: 

588 cudaError_t _static_cudaGraphMemcpyNodeSetParams1D "cudaGraphMemcpyNodeSetParams1D" (cudaGraphNode_t node, void* dst, const void* src, size_t count, cudaMemcpyKind kind) noexcept 

589  

590cdef extern from 'cuda_runtime_api.h' nogil: 

591 cudaError_t _static_cudaGraphAddMemsetNode "cudaGraphAddMemsetNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaMemsetParams* pMemsetParams) noexcept 

592  

593cdef extern from 'cuda_runtime_api.h' nogil: 

594 cudaError_t _static_cudaGraphMemsetNodeGetParams "cudaGraphMemsetNodeGetParams" (cudaGraphNode_t node, cudaMemsetParams* pNodeParams) noexcept 

595  

596cdef extern from 'cuda_runtime_api.h' nogil: 

597 cudaError_t _static_cudaGraphMemsetNodeSetParams "cudaGraphMemsetNodeSetParams" (cudaGraphNode_t node, const cudaMemsetParams* pNodeParams) noexcept 

598  

599cdef extern from 'cuda_runtime_api.h' nogil: 

600 cudaError_t _static_cudaGraphAddHostNode "cudaGraphAddHostNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaHostNodeParams* pNodeParams) noexcept 

601  

602cdef extern from 'cuda_runtime_api.h' nogil: 

603 cudaError_t _static_cudaGraphHostNodeGetParams "cudaGraphHostNodeGetParams" (cudaGraphNode_t node, cudaHostNodeParams* pNodeParams) noexcept 

604  

605cdef extern from 'cuda_runtime_api.h' nogil: 

606 cudaError_t _static_cudaGraphHostNodeSetParams "cudaGraphHostNodeSetParams" (cudaGraphNode_t node, const cudaHostNodeParams* pNodeParams) noexcept 

607  

608cdef extern from 'cuda_runtime_api.h' nogil: 

609 cudaError_t _static_cudaGraphAddChildGraphNode "cudaGraphAddChildGraphNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaGraph_t childGraph) noexcept 

610  

611cdef extern from 'cuda_runtime_api.h' nogil: 

612 cudaError_t _static_cudaGraphChildGraphNodeGetGraph "cudaGraphChildGraphNodeGetGraph" (cudaGraphNode_t node, cudaGraph_t* pGraph) noexcept 

613  

614cdef extern from 'cuda_runtime_api.h' nogil: 

615 cudaError_t _static_cudaGraphAddEmptyNode "cudaGraphAddEmptyNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies) noexcept 

616  

617cdef extern from 'cuda_runtime_api.h' nogil: 

618 cudaError_t _static_cudaGraphAddEventRecordNode "cudaGraphAddEventRecordNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaEvent_t event) noexcept 

619  

620cdef extern from 'cuda_runtime_api.h' nogil: 

621 cudaError_t _static_cudaGraphEventRecordNodeGetEvent "cudaGraphEventRecordNodeGetEvent" (cudaGraphNode_t node, cudaEvent_t* event_out) noexcept 

622  

623cdef extern from 'cuda_runtime_api.h' nogil: 

624 cudaError_t _static_cudaGraphEventRecordNodeSetEvent "cudaGraphEventRecordNodeSetEvent" (cudaGraphNode_t node, cudaEvent_t event) noexcept 

625  

626cdef extern from 'cuda_runtime_api.h' nogil: 

627 cudaError_t _static_cudaGraphAddEventWaitNode "cudaGraphAddEventWaitNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaEvent_t event) noexcept 

628  

629cdef extern from 'cuda_runtime_api.h' nogil: 

630 cudaError_t _static_cudaGraphEventWaitNodeGetEvent "cudaGraphEventWaitNodeGetEvent" (cudaGraphNode_t node, cudaEvent_t* event_out) noexcept 

631  

632cdef extern from 'cuda_runtime_api.h' nogil: 

633 cudaError_t _static_cudaGraphEventWaitNodeSetEvent "cudaGraphEventWaitNodeSetEvent" (cudaGraphNode_t node, cudaEvent_t event) noexcept 

634  

635cdef extern from 'cuda_runtime_api.h' nogil: 

636 cudaError_t _static_cudaGraphAddExternalSemaphoresSignalNode "cudaGraphAddExternalSemaphoresSignalNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaExternalSemaphoreSignalNodeParams* nodeParams) noexcept 

637  

638cdef extern from 'cuda_runtime_api.h' nogil: 

639 cudaError_t _static_cudaGraphExternalSemaphoresSignalNodeGetParams "cudaGraphExternalSemaphoresSignalNodeGetParams" (cudaGraphNode_t hNode, cudaExternalSemaphoreSignalNodeParams* params_out) noexcept 

640  

641cdef extern from 'cuda_runtime_api.h' nogil: 

642 cudaError_t _static_cudaGraphExternalSemaphoresSignalNodeSetParams "cudaGraphExternalSemaphoresSignalNodeSetParams" (cudaGraphNode_t hNode, const cudaExternalSemaphoreSignalNodeParams* nodeParams) noexcept 

643  

644cdef extern from 'cuda_runtime_api.h' nogil: 

645 cudaError_t _static_cudaGraphAddExternalSemaphoresWaitNode "cudaGraphAddExternalSemaphoresWaitNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaExternalSemaphoreWaitNodeParams* nodeParams) noexcept 

646  

647cdef extern from 'cuda_runtime_api.h' nogil: 

648 cudaError_t _static_cudaGraphExternalSemaphoresWaitNodeGetParams "cudaGraphExternalSemaphoresWaitNodeGetParams" (cudaGraphNode_t hNode, cudaExternalSemaphoreWaitNodeParams* params_out) noexcept 

649  

650cdef extern from 'cuda_runtime_api.h' nogil: 

651 cudaError_t _static_cudaGraphExternalSemaphoresWaitNodeSetParams "cudaGraphExternalSemaphoresWaitNodeSetParams" (cudaGraphNode_t hNode, const cudaExternalSemaphoreWaitNodeParams* nodeParams) noexcept 

652  

653cdef extern from 'cuda_runtime_api.h' nogil: 

654 cudaError_t _static_cudaGraphAddMemAllocNode "cudaGraphAddMemAllocNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaMemAllocNodeParams* nodeParams) noexcept 

655  

656cdef extern from 'cuda_runtime_api.h' nogil: 

657 cudaError_t _static_cudaGraphMemAllocNodeGetParams "cudaGraphMemAllocNodeGetParams" (cudaGraphNode_t node, cudaMemAllocNodeParams* params_out) noexcept 

658  

659cdef extern from 'cuda_runtime_api.h' nogil: 

660 cudaError_t _static_cudaGraphAddMemFreeNode "cudaGraphAddMemFreeNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, void* dptr) noexcept 

661  

662cdef extern from 'cuda_runtime_api.h' nogil: 

663 cudaError_t _static_cudaGraphMemFreeNodeGetParams "cudaGraphMemFreeNodeGetParams" (cudaGraphNode_t node, void* dptr_out) noexcept 

664  

665cdef extern from 'cuda_runtime_api.h' nogil: 

666 cudaError_t _static_cudaDeviceGraphMemTrim "cudaDeviceGraphMemTrim" (int device) noexcept 

667  

668cdef extern from 'cuda_runtime_api.h' nogil: 

669 cudaError_t _static_cudaDeviceGetGraphMemAttribute "cudaDeviceGetGraphMemAttribute" (int device, cudaGraphMemAttributeType attr, void* value) noexcept 

670  

671cdef extern from 'cuda_runtime_api.h' nogil: 

672 cudaError_t _static_cudaDeviceSetGraphMemAttribute "cudaDeviceSetGraphMemAttribute" (int device, cudaGraphMemAttributeType attr, void* value) noexcept 

673  

674cdef extern from 'cuda_runtime_api.h' nogil: 

675 cudaError_t _static_cudaGraphClone "cudaGraphClone" (cudaGraph_t* pGraphClone, cudaGraph_t originalGraph) noexcept 

676  

677cdef extern from 'cuda_runtime_api.h' nogil: 

678 cudaError_t _static_cudaGraphNodeFindInClone "cudaGraphNodeFindInClone" (cudaGraphNode_t* pNode, cudaGraphNode_t originalNode, cudaGraph_t clonedGraph) noexcept 

679  

680cdef extern from 'cuda_runtime_api.h' nogil: 

681 cudaError_t _static_cudaGraphNodeGetType "cudaGraphNodeGetType" (cudaGraphNode_t node, cudaGraphNodeType* pType) noexcept 

682  

683cdef extern from 'cuda_runtime_api.h' nogil: 

684 cudaError_t _static_cudaGraphGetNodes "cudaGraphGetNodes" (cudaGraph_t graph, cudaGraphNode_t* nodes, size_t* numNodes) noexcept 

685  

686cdef extern from 'cuda_runtime_api.h' nogil: 

687 cudaError_t _static_cudaGraphGetRootNodes "cudaGraphGetRootNodes" (cudaGraph_t graph, cudaGraphNode_t* pRootNodes, size_t* pNumRootNodes) noexcept 

688  

689cdef extern from 'cuda_runtime_api.h' nogil: 

690 cudaError_t _static_cudaGraphGetEdges "cudaGraphGetEdges" (cudaGraph_t graph, cudaGraphNode_t* from_, cudaGraphNode_t* to, cudaGraphEdgeData* edgeData, size_t* numEdges) noexcept 

691  

692cdef extern from 'cuda_runtime_api.h' nogil: 

693 cudaError_t _static_cudaGraphNodeGetDependencies "cudaGraphNodeGetDependencies" (cudaGraphNode_t node, cudaGraphNode_t* pDependencies, cudaGraphEdgeData* edgeData, size_t* pNumDependencies) noexcept 

694  

695cdef extern from 'cuda_runtime_api.h' nogil: 

696 cudaError_t _static_cudaGraphNodeGetDependentNodes "cudaGraphNodeGetDependentNodes" (cudaGraphNode_t node, cudaGraphNode_t* pDependentNodes, cudaGraphEdgeData* edgeData, size_t* pNumDependentNodes) noexcept 

697  

698cdef extern from 'cuda_runtime_api.h' nogil: 

699 cudaError_t _static_cudaGraphAddDependencies "cudaGraphAddDependencies" (cudaGraph_t graph, const cudaGraphNode_t* from_, const cudaGraphNode_t* to, const cudaGraphEdgeData* edgeData, size_t numDependencies) noexcept 

700  

701cdef extern from 'cuda_runtime_api.h' nogil: 

702 cudaError_t _static_cudaGraphRemoveDependencies "cudaGraphRemoveDependencies" (cudaGraph_t graph, const cudaGraphNode_t* from_, const cudaGraphNode_t* to, const cudaGraphEdgeData* edgeData, size_t numDependencies) noexcept 

703  

704cdef extern from 'cuda_runtime_api.h' nogil: 

705 cudaError_t _static_cudaGraphDestroyNode "cudaGraphDestroyNode" (cudaGraphNode_t node) noexcept 

706  

707cdef extern from 'cuda_runtime_api.h' nogil: 

708 cudaError_t _static_cudaGraphInstantiate "cudaGraphInstantiate" (cudaGraphExec_t* pGraphExec, cudaGraph_t graph, unsigned long long flags) noexcept 

709  

710cdef extern from 'cuda_runtime_api.h' nogil: 

711 cudaError_t _static_cudaGraphInstantiateWithFlags "cudaGraphInstantiateWithFlags" (cudaGraphExec_t* pGraphExec, cudaGraph_t graph, unsigned long long flags) noexcept 

712  

713cdef extern from 'cuda_runtime_api.h' nogil: 

714 cudaError_t _static_cudaGraphInstantiateWithParams "cudaGraphInstantiateWithParams" (cudaGraphExec_t* pGraphExec, cudaGraph_t graph, cudaGraphInstantiateParams* instantiateParams) noexcept 

715  

716cdef extern from 'cuda_runtime_api.h' nogil: 

717 cudaError_t _static_cudaGraphExecGetFlags "cudaGraphExecGetFlags" (cudaGraphExec_t graphExec, unsigned long long* flags) noexcept 

718  

719cdef extern from 'cuda_runtime_api.h' nogil: 

720 cudaError_t _static_cudaGraphExecKernelNodeSetParams "cudaGraphExecKernelNodeSetParams" (cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaKernelNodeParams* pNodeParams) noexcept 

721  

722cdef extern from 'cuda_runtime_api.h' nogil: 

723 cudaError_t _static_cudaGraphExecMemcpyNodeSetParams "cudaGraphExecMemcpyNodeSetParams" (cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaMemcpy3DParms* pNodeParams) noexcept 

724  

725cdef extern from 'cuda_runtime_api.h' nogil: 

726 cudaError_t _static_cudaGraphExecMemcpyNodeSetParams1D "cudaGraphExecMemcpyNodeSetParams1D" (cudaGraphExec_t hGraphExec, cudaGraphNode_t node, void* dst, const void* src, size_t count, cudaMemcpyKind kind) noexcept 

727  

728cdef extern from 'cuda_runtime_api.h' nogil: 

729 cudaError_t _static_cudaGraphExecMemsetNodeSetParams "cudaGraphExecMemsetNodeSetParams" (cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaMemsetParams* pNodeParams) noexcept 

730  

731cdef extern from 'cuda_runtime_api.h' nogil: 

732 cudaError_t _static_cudaGraphExecHostNodeSetParams "cudaGraphExecHostNodeSetParams" (cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaHostNodeParams* pNodeParams) noexcept 

733  

734cdef extern from 'cuda_runtime_api.h' nogil: 

735 cudaError_t _static_cudaGraphExecChildGraphNodeSetParams "cudaGraphExecChildGraphNodeSetParams" (cudaGraphExec_t hGraphExec, cudaGraphNode_t node, cudaGraph_t childGraph) noexcept 

736  

737cdef extern from 'cuda_runtime_api.h' nogil: 

738 cudaError_t _static_cudaGraphExecEventRecordNodeSetEvent "cudaGraphExecEventRecordNodeSetEvent" (cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, cudaEvent_t event) noexcept 

739  

740cdef extern from 'cuda_runtime_api.h' nogil: 

741 cudaError_t _static_cudaGraphExecEventWaitNodeSetEvent "cudaGraphExecEventWaitNodeSetEvent" (cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, cudaEvent_t event) noexcept 

742  

743cdef extern from 'cuda_runtime_api.h' nogil: 

744 cudaError_t _static_cudaGraphExecExternalSemaphoresSignalNodeSetParams "cudaGraphExecExternalSemaphoresSignalNodeSetParams" (cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, const cudaExternalSemaphoreSignalNodeParams* nodeParams) noexcept 

745  

746cdef extern from 'cuda_runtime_api.h' nogil: 

747 cudaError_t _static_cudaGraphExecExternalSemaphoresWaitNodeSetParams "cudaGraphExecExternalSemaphoresWaitNodeSetParams" (cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, const cudaExternalSemaphoreWaitNodeParams* nodeParams) noexcept 

748  

749cdef extern from 'cuda_runtime_api.h' nogil: 

750 cudaError_t _static_cudaGraphNodeSetEnabled "cudaGraphNodeSetEnabled" (cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, unsigned int isEnabled) noexcept 

751  

752cdef extern from 'cuda_runtime_api.h' nogil: 

753 cudaError_t _static_cudaGraphNodeGetEnabled "cudaGraphNodeGetEnabled" (cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, unsigned int* isEnabled) noexcept 

754  

755cdef extern from 'cuda_runtime_api.h' nogil: 

756 cudaError_t _static_cudaGraphExecUpdate "cudaGraphExecUpdate" (cudaGraphExec_t hGraphExec, cudaGraph_t hGraph, cudaGraphExecUpdateResultInfo* resultInfo) noexcept 

757  

758cdef extern from 'cuda_runtime_api.h' nogil: 

759 cudaError_t _static_cudaGraphUpload "cudaGraphUpload" (cudaGraphExec_t graphExec, cudaStream_t stream) noexcept 

760  

761cdef extern from 'cuda_runtime_api.h' nogil: 

762 cudaError_t _static_cudaGraphLaunch "cudaGraphLaunch" (cudaGraphExec_t graphExec, cudaStream_t stream) noexcept 

763  

764cdef extern from 'cuda_runtime_api.h' nogil: 

765 cudaError_t _static_cudaGraphExecDestroy "cudaGraphExecDestroy" (cudaGraphExec_t graphExec) noexcept 

766  

767cdef extern from 'cuda_runtime_api.h' nogil: 

768 cudaError_t _static_cudaGraphDestroy "cudaGraphDestroy" (cudaGraph_t graph) noexcept 

769  

770cdef extern from 'cuda_runtime_api.h' nogil: 

771 cudaError_t _static_cudaGraphDebugDotPrint "cudaGraphDebugDotPrint" (cudaGraph_t graph, const char* path, unsigned int flags) noexcept 

772  

773cdef extern from 'cuda_runtime_api.h' nogil: 

774 cudaError_t _static_cudaUserObjectCreate "cudaUserObjectCreate" (cudaUserObject_t* object_out, void* ptr, cudaHostFn_t destroy, unsigned int initialRefcount, unsigned int flags) noexcept 

775  

776cdef extern from 'cuda_runtime_api.h' nogil: 

777 cudaError_t _static_cudaUserObjectRetain "cudaUserObjectRetain" (cudaUserObject_t object, unsigned int count) noexcept 

778  

779cdef extern from 'cuda_runtime_api.h' nogil: 

780 cudaError_t _static_cudaUserObjectRelease "cudaUserObjectRelease" (cudaUserObject_t object, unsigned int count) noexcept 

781  

782cdef extern from 'cuda_runtime_api.h' nogil: 

783 cudaError_t _static_cudaGraphRetainUserObject "cudaGraphRetainUserObject" (cudaGraph_t graph, cudaUserObject_t object, unsigned int count, unsigned int flags) noexcept 

784  

785cdef extern from 'cuda_runtime_api.h' nogil: 

786 cudaError_t _static_cudaGraphReleaseUserObject "cudaGraphReleaseUserObject" (cudaGraph_t graph, cudaUserObject_t object, unsigned int count) noexcept 

787  

788cdef extern from 'cuda_runtime_api.h' nogil: 

789 cudaError_t _static_cudaGraphAddNode "cudaGraphAddNode" (cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, const cudaGraphEdgeData* dependencyData, size_t numDependencies, cudaGraphNodeParams* nodeParams) noexcept 

790  

791cdef extern from 'cuda_runtime_api.h' nogil: 

792 cudaError_t _static_cudaGraphNodeSetParams "cudaGraphNodeSetParams" (cudaGraphNode_t node, cudaGraphNodeParams* nodeParams) noexcept 

793  

794cdef extern from 'cuda_runtime_api.h' nogil: 

795 cudaError_t _static_cudaGraphExecNodeSetParams "cudaGraphExecNodeSetParams" (cudaGraphExec_t graphExec, cudaGraphNode_t node, cudaGraphNodeParams* nodeParams) noexcept 

796  

797cdef extern from 'cuda_runtime_api.h' nogil: 

798 cudaError_t _static_cudaGraphConditionalHandleCreate "cudaGraphConditionalHandleCreate" (cudaGraphConditionalHandle* pHandle_out, cudaGraph_t graph, unsigned int defaultLaunchValue, unsigned int flags) noexcept 

799  

800cdef extern from 'cuda_runtime_api.h' nogil: 

801 cudaError_t _static_cudaGetDriverEntryPoint "cudaGetDriverEntryPoint" (const char* symbol, void** funcPtr, unsigned long long flags, cudaDriverEntryPointQueryResult* driverStatus) noexcept 

802  

803cdef extern from 'cuda_runtime_api.h' nogil: 

804 cudaError_t _static_cudaGetDriverEntryPointByVersion "cudaGetDriverEntryPointByVersion" (const char* symbol, void** funcPtr, unsigned int cudaVersion, unsigned long long flags, cudaDriverEntryPointQueryResult* driverStatus) noexcept 

805  

806cdef extern from 'cuda_runtime_api.h' nogil: 

807 cudaError_t _static_cudaLibraryLoadData "cudaLibraryLoadData" (cudaLibrary_t* library, const void* code, cudaJitOption* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, cudaLibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) noexcept 

808  

809cdef extern from 'cuda_runtime_api.h' nogil: 

810 cudaError_t _static_cudaLibraryLoadFromFile "cudaLibraryLoadFromFile" (cudaLibrary_t* library, const char* fileName, cudaJitOption* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, cudaLibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) noexcept 

811  

812cdef extern from 'cuda_runtime_api.h' nogil: 

813 cudaError_t _static_cudaLibraryUnload "cudaLibraryUnload" (cudaLibrary_t library) noexcept 

814  

815cdef extern from 'cuda_runtime_api.h' nogil: 

816 cudaError_t _static_cudaLibraryGetKernel "cudaLibraryGetKernel" (cudaKernel_t* pKernel, cudaLibrary_t library, const char* name) noexcept 

817  

818cdef extern from 'cuda_runtime_api.h' nogil: 

819 cudaError_t _static_cudaLibraryGetGlobal "cudaLibraryGetGlobal" (void** dptr, size_t* bytes, cudaLibrary_t library, const char* name) noexcept 

820  

821cdef extern from 'cuda_runtime_api.h' nogil: 

822 cudaError_t _static_cudaLibraryGetManaged "cudaLibraryGetManaged" (void** dptr, size_t* bytes, cudaLibrary_t library, const char* name) noexcept 

823  

824cdef extern from 'cuda_runtime_api.h' nogil: 

825 cudaError_t _static_cudaLibraryGetUnifiedFunction "cudaLibraryGetUnifiedFunction" (void** fptr, cudaLibrary_t library, const char* symbol) noexcept 

826  

827cdef extern from 'cuda_runtime_api.h' nogil: 

828 cudaError_t _static_cudaLibraryGetKernelCount "cudaLibraryGetKernelCount" (unsigned int* count, cudaLibrary_t lib) noexcept 

829  

830cdef extern from 'cuda_runtime_api.h' nogil: 

831 cudaError_t _static_cudaLibraryEnumerateKernels "cudaLibraryEnumerateKernels" (cudaKernel_t* kernels, unsigned int numKernels, cudaLibrary_t lib) noexcept 

832  

833cdef extern from 'cuda_runtime_api.h' nogil: 

834 cudaError_t _static_cudaKernelSetAttributeForDevice "cudaKernelSetAttributeForDevice" (cudaKernel_t kernel, cudaFuncAttribute attr, int value, int device) noexcept 

835  

836cdef extern from 'cuda_runtime_api.h' nogil: 

837 cudaError_t _static_cudaGetExportTable "cudaGetExportTable" (const void** ppExportTable, const cudaUUID_t* pExportTableId) noexcept 

838  

839cdef extern from 'cuda_runtime_api.h' nogil: 

840 cudaError_t _static_cudaGetKernel "cudaGetKernel" (cudaKernel_t* kernelPtr, const void* entryFuncAddr) noexcept 

841  

842cdef extern from 'cuda_profiler_api.h' nogil: 

843 cudaError_t _static_cudaProfilerStart "cudaProfilerStart" () noexcept 

844  

845cdef extern from 'cuda_profiler_api.h' nogil: 

846 cudaError_t _static_cudaProfilerStop "cudaProfilerStop" () noexcept 

847  

848cdef extern from 'cuda_runtime_api.h' nogil: 

849 cudaError_t _static_cudaGetDeviceProperties "cudaGetDeviceProperties" (cudaDeviceProp* prop, int device) noexcept 

850  

851cdef extern from 'cuda_runtime_api.h' nogil: 

852 cudaError_t _static_cudaDeviceGetHostAtomicCapabilities "cudaDeviceGetHostAtomicCapabilities" (unsigned int* capabilities, const cudaAtomicOperation* operations, unsigned int count, int device) noexcept 

853  

854cdef extern from 'cuda_runtime_api.h' nogil: 

855 cudaError_t _static_cudaDeviceGetP2PAtomicCapabilities "cudaDeviceGetP2PAtomicCapabilities" (unsigned int* capabilities, const cudaAtomicOperation* operations, unsigned int count, int srcDevice, int dstDevice) noexcept 

856  

857cdef extern from 'cuda_runtime_api.h' nogil: 

858 cudaError_t _static_cudaStreamGetCaptureInfo "cudaStreamGetCaptureInfo" (cudaStream_t stream, cudaStreamCaptureStatus* captureStatus_out, unsigned long long* id_out, cudaGraph_t* graph_out, const cudaGraphNode_t** dependencies_out, const cudaGraphEdgeData** edgeData_out, size_t* numDependencies_out) noexcept 

859  

860cdef extern from 'cuda_runtime_api.h' nogil: 

861 cudaError_t _static_cudaSignalExternalSemaphoresAsync "cudaSignalExternalSemaphoresAsync" (const cudaExternalSemaphore_t* extSemArray, const cudaExternalSemaphoreSignalParams* paramsArray, unsigned int numExtSems, cudaStream_t stream) noexcept 

862  

863cdef extern from 'cuda_runtime_api.h' nogil: 

864 cudaError_t _static_cudaWaitExternalSemaphoresAsync "cudaWaitExternalSemaphoresAsync" (const cudaExternalSemaphore_t* extSemArray, const cudaExternalSemaphoreWaitParams* paramsArray, unsigned int numExtSems, cudaStream_t stream) noexcept 

865  

866cdef extern from 'cuda_runtime_api.h' nogil: 

867 cudaError_t _static_cudaMemPrefetchBatchAsync "cudaMemPrefetchBatchAsync" (void** dptrs, size_t* sizes, size_t count, cudaMemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, cudaStream_t stream) noexcept 

868  

869cdef extern from 'cuda_runtime_api.h' nogil: 

870 cudaError_t _static_cudaMemDiscardBatchAsync "cudaMemDiscardBatchAsync" (void** dptrs, size_t* sizes, size_t count, unsigned long long flags, cudaStream_t stream) noexcept 

871  

872cdef extern from 'cuda_runtime_api.h' nogil: 

873 cudaError_t _static_cudaMemDiscardAndPrefetchBatchAsync "cudaMemDiscardAndPrefetchBatchAsync" (void** dptrs, size_t* sizes, size_t count, cudaMemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, cudaStream_t stream) noexcept 

874  

875cdef extern from 'cuda_runtime_api.h' nogil: 

876 cudaError_t _static_cudaMemGetDefaultMemPool "cudaMemGetDefaultMemPool" (cudaMemPool_t* memPool, cudaMemLocation* location, cudaMemAllocationType type) noexcept 

877  

878cdef extern from 'cuda_runtime_api.h' nogil: 

879 cudaError_t _static_cudaMemGetMemPool "cudaMemGetMemPool" (cudaMemPool_t* memPool, cudaMemLocation* location, cudaMemAllocationType type) noexcept 

880  

881cdef extern from 'cuda_runtime_api.h' nogil: 

882 cudaError_t _static_cudaMemSetMemPool "cudaMemSetMemPool" (cudaMemLocation* location, cudaMemAllocationType type, cudaMemPool_t memPool) noexcept 

883  

884cdef extern from 'cuda_runtime_api.h' nogil: 

885 cudaError_t _static_cudaLogsRegisterCallback "cudaLogsRegisterCallback" (cudaLogsCallback_t callbackFunc, void* userData, cudaLogsCallbackHandle* callback_out) noexcept 

886  

887cdef extern from 'cuda_runtime_api.h' nogil: 

888 cudaError_t _static_cudaLogsUnregisterCallback "cudaLogsUnregisterCallback" (cudaLogsCallbackHandle callback) noexcept 

889  

890cdef extern from 'cuda_runtime_api.h' nogil: 

891 cudaError_t _static_cudaLogsCurrent "cudaLogsCurrent" (cudaLogIterator* iterator_out, unsigned int flags) noexcept 

892  

893cdef extern from 'cuda_runtime_api.h' nogil: 

894 cudaError_t _static_cudaLogsDumpToFile "cudaLogsDumpToFile" (cudaLogIterator* iterator, const char* pathToFile, unsigned int flags) noexcept 

895  

896cdef extern from 'cuda_runtime_api.h' nogil: 

897 cudaError_t _static_cudaLogsDumpToMemory "cudaLogsDumpToMemory" (cudaLogIterator* iterator, char* buffer, size_t* size, unsigned int flags) noexcept 

898  

899cdef extern from 'cuda_runtime_api.h' nogil: 

900 cudaError_t _static_cudaGraphNodeGetContainingGraph "cudaGraphNodeGetContainingGraph" (cudaGraphNode_t hNode, cudaGraph_t* phGraph) noexcept 

901  

902cdef extern from 'cuda_runtime_api.h' nogil: 

903 cudaError_t _static_cudaGraphNodeGetLocalId "cudaGraphNodeGetLocalId" (cudaGraphNode_t hNode, unsigned int* nodeId) noexcept 

904  

905cdef extern from 'cuda_runtime_api.h' nogil: 

906 cudaError_t _static_cudaGraphNodeGetToolsId "cudaGraphNodeGetToolsId" (cudaGraphNode_t hNode, unsigned long long* toolsNodeId) noexcept 

907  

908cdef extern from 'cuda_runtime_api.h' nogil: 

909 cudaError_t _static_cudaGraphGetId "cudaGraphGetId" (cudaGraph_t hGraph, unsigned int* graphID) noexcept 

910  

911cdef extern from 'cuda_runtime_api.h' nogil: 

912 cudaError_t _static_cudaGraphExecGetId "cudaGraphExecGetId" (cudaGraphExec_t hGraphExec, unsigned int* graphID) noexcept 

913  

914cdef extern from 'cuda_runtime_api.h' nogil: 

915 cudaError_t _static_cudaGraphConditionalHandleCreate_v2 "cudaGraphConditionalHandleCreate_v2" (cudaGraphConditionalHandle* pHandle_out, cudaGraph_t graph, cudaExecutionContext_t ctx, unsigned int defaultLaunchValue, unsigned int flags) noexcept 

916  

917cdef extern from 'cuda_runtime_api.h' nogil: 

918 cudaError_t _static_cudaDeviceGetDevResource "cudaDeviceGetDevResource" (int device, cudaDevResource* resource, cudaDevResourceType type) noexcept 

919  

920cdef extern from 'cuda_runtime_api.h' nogil: 

921 cudaError_t _static_cudaDevSmResourceSplitByCount "cudaDevSmResourceSplitByCount" (cudaDevResource* result, unsigned int* nbGroups, const cudaDevResource* input, cudaDevResource* remaining, unsigned int flags, unsigned int minCount) noexcept 

922  

923cdef extern from 'cuda_runtime_api.h' nogil: 

924 cudaError_t _static_cudaDevSmResourceSplit "cudaDevSmResourceSplit" (cudaDevResource* result, unsigned int nbGroups, const cudaDevResource* input, cudaDevResource* remainder, unsigned int flags, cudaDevSmResourceGroupParams* groupParams) noexcept 

925  

926cdef extern from 'cuda_runtime_api.h' nogil: 

927 cudaError_t _static_cudaDevResourceGenerateDesc "cudaDevResourceGenerateDesc" (cudaDevResourceDesc_t* phDesc, cudaDevResource* resources, unsigned int nbResources) noexcept 

928  

929cdef extern from 'cuda_runtime_api.h' nogil: 

930 cudaError_t _static_cudaGreenCtxCreate "cudaGreenCtxCreate" (cudaExecutionContext_t* phCtx, cudaDevResourceDesc_t desc, int device, unsigned int flags) noexcept 

931  

932cdef extern from 'cuda_runtime_api.h' nogil: 

933 cudaError_t _static_cudaExecutionCtxDestroy "cudaExecutionCtxDestroy" (cudaExecutionContext_t ctx) noexcept 

934  

935cdef extern from 'cuda_runtime_api.h' nogil: 

936 cudaError_t _static_cudaExecutionCtxGetDevResource "cudaExecutionCtxGetDevResource" (cudaExecutionContext_t ctx, cudaDevResource* resource, cudaDevResourceType type) noexcept 

937  

938cdef extern from 'cuda_runtime_api.h' nogil: 

939 cudaError_t _static_cudaExecutionCtxGetDevice "cudaExecutionCtxGetDevice" (int* device, cudaExecutionContext_t ctx) noexcept 

940  

941cdef extern from 'cuda_runtime_api.h' nogil: 

942 cudaError_t _static_cudaExecutionCtxGetId "cudaExecutionCtxGetId" (cudaExecutionContext_t ctx, unsigned long long* ctxId) noexcept 

943  

944cdef extern from 'cuda_runtime_api.h' nogil: 

945 cudaError_t _static_cudaExecutionCtxStreamCreate "cudaExecutionCtxStreamCreate" (cudaStream_t* phStream, cudaExecutionContext_t ctx, unsigned int flags, int priority) noexcept 

946  

947cdef extern from 'cuda_runtime_api.h' nogil: 

948 cudaError_t _static_cudaExecutionCtxSynchronize "cudaExecutionCtxSynchronize" (cudaExecutionContext_t ctx) noexcept 

949  

950cdef extern from 'cuda_runtime_api.h' nogil: 

951 cudaError_t _static_cudaStreamGetDevResource "cudaStreamGetDevResource" (cudaStream_t hStream, cudaDevResource* resource, cudaDevResourceType type) noexcept 

952  

953cdef extern from 'cuda_runtime_api.h' nogil: 

954 cudaError_t _static_cudaExecutionCtxRecordEvent "cudaExecutionCtxRecordEvent" (cudaExecutionContext_t ctx, cudaEvent_t event) noexcept 

955  

956cdef extern from 'cuda_runtime_api.h' nogil: 

957 cudaError_t _static_cudaExecutionCtxWaitEvent "cudaExecutionCtxWaitEvent" (cudaExecutionContext_t ctx, cudaEvent_t event) noexcept 

958  

959cdef extern from 'cuda_runtime_api.h' nogil: 

960 cudaError_t _static_cudaDeviceGetExecutionCtx "cudaDeviceGetExecutionCtx" (cudaExecutionContext_t* ctx, int device) noexcept 

961  

962cdef extern from 'cuda_runtime_api.h' nogil: 

963 cudaError_t _static_cudaFuncGetParamCount "cudaFuncGetParamCount" (const void* func, size_t* paramCount) noexcept 

964  

965cdef extern from 'cuda_runtime_api.h' nogil: 

966 cudaError_t _static_cudaLaunchHostFunc_v2 "cudaLaunchHostFunc_v2" (cudaStream_t stream, cudaHostFn_t fn, void* userData, unsigned int syncMode) noexcept 

967  

968cdef extern from 'cuda_runtime_api.h' nogil: 

969 cudaError_t _static_cudaMemcpyWithAttributesAsync "cudaMemcpyWithAttributesAsync" (void* dst, const void* src, size_t size, cudaMemcpyAttributes* attr, cudaStream_t stream) noexcept 

970  

971cdef extern from 'cuda_runtime_api.h' nogil: 

972 cudaError_t _static_cudaMemcpy3DWithAttributesAsync "cudaMemcpy3DWithAttributesAsync" (cudaMemcpy3DBatchOp* op, unsigned long long flags, cudaStream_t stream) noexcept 

973  

974cdef extern from 'cuda_runtime_api.h' nogil: 

975 cudaError_t _static_cudaGraphNodeGetParams "cudaGraphNodeGetParams" (cudaGraphNode_t node, cudaGraphNodeParams* nodeParams) noexcept 

976  

977cdef extern from 'cuda_runtime_api.h' nogil: 

978 cudaError_t _static_cudaStreamBeginRecaptureToGraph "cudaStreamBeginRecaptureToGraph" (cudaStream_t stream, cudaStreamCaptureMode mode, cudaGraph_t graph, cudaGraphRecaptureCallbackData* callbackData) noexcept 

979  

980  

981############################################################################### 

982# Wrapper functions 

983############################################################################### 

984  

985cdef cudaError_t _cudaDeviceReset() except ?cudaErrorCallRequiresNewerDriver nogil: 

986 return _static_cudaDeviceReset() 

987  

988  

989cdef cudaError_t _cudaDeviceSynchronize() except ?cudaErrorCallRequiresNewerDriver nogil: 

990 return _static_cudaDeviceSynchronize() 

991  

992  

993cdef cudaError_t _cudaDeviceSetLimit(cudaLimit limit, size_t value) except ?cudaErrorCallRequiresNewerDriver nogil: 

994 return _static_cudaDeviceSetLimit(limit, value) 

995  

996  

997cdef cudaError_t _cudaDeviceGetLimit(size_t* pValue, cudaLimit limit) except ?cudaErrorCallRequiresNewerDriver nogil: 

998 return _static_cudaDeviceGetLimit(pValue, limit) 

999  

1000  

1001cdef cudaError_t _cudaDeviceGetTexture1DLinearMaxWidth(size_t* maxWidthInElements, const cudaChannelFormatDesc* fmtDesc, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1002 return _static_cudaDeviceGetTexture1DLinearMaxWidth(maxWidthInElements, fmtDesc, device) 

1003  

1004  

1005cdef cudaError_t _cudaDeviceGetCacheConfig(cudaFuncCache* pCacheConfig) except ?cudaErrorCallRequiresNewerDriver nogil: 

1006 return _static_cudaDeviceGetCacheConfig(pCacheConfig) 

1007  

1008  

1009cdef cudaError_t _cudaDeviceGetStreamPriorityRange(int* leastPriority, int* greatestPriority) except ?cudaErrorCallRequiresNewerDriver nogil: 

1010 return _static_cudaDeviceGetStreamPriorityRange(leastPriority, greatestPriority) 

1011  

1012  

1013cdef cudaError_t _cudaDeviceSetCacheConfig(cudaFuncCache cacheConfig) except ?cudaErrorCallRequiresNewerDriver nogil: 

1014 return _static_cudaDeviceSetCacheConfig(cacheConfig) 

1015  

1016  

1017cdef cudaError_t _cudaDeviceGetByPCIBusId(int* device, const char* pciBusId) except ?cudaErrorCallRequiresNewerDriver nogil: 

1018 return _static_cudaDeviceGetByPCIBusId(device, pciBusId) 

1019  

1020  

1021cdef cudaError_t _cudaDeviceGetPCIBusId(char* pciBusId, int len, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1022 return _static_cudaDeviceGetPCIBusId(pciBusId, len, device) 

1023  

1024  

1025cdef cudaError_t _cudaIpcGetEventHandle(cudaIpcEventHandle_t* handle, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1026 return _static_cudaIpcGetEventHandle(handle, event) 

1027  

1028  

1029cdef cudaError_t _cudaIpcOpenEventHandle(cudaEvent_t* event, cudaIpcEventHandle_t handle) except ?cudaErrorCallRequiresNewerDriver nogil: 

1030 return _static_cudaIpcOpenEventHandle(event, handle) 

1031  

1032  

1033cdef cudaError_t _cudaIpcGetMemHandle(cudaIpcMemHandle_t* handle, void* devPtr) except ?cudaErrorCallRequiresNewerDriver nogil: 

1034 return _static_cudaIpcGetMemHandle(handle, devPtr) 

1035  

1036  

1037cdef cudaError_t _cudaIpcOpenMemHandle(void** devPtr, cudaIpcMemHandle_t handle, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1038 return _static_cudaIpcOpenMemHandle(devPtr, handle, flags) 

1039  

1040  

1041cdef cudaError_t _cudaIpcCloseMemHandle(void* devPtr) except ?cudaErrorCallRequiresNewerDriver nogil: 

1042 return _static_cudaIpcCloseMemHandle(devPtr) 

1043  

1044  

1045cdef cudaError_t _cudaDeviceFlushGPUDirectRDMAWrites(cudaFlushGPUDirectRDMAWritesTarget target, cudaFlushGPUDirectRDMAWritesScope scope) except ?cudaErrorCallRequiresNewerDriver nogil: 

1046 return _static_cudaDeviceFlushGPUDirectRDMAWrites(target, scope) 

1047  

1048  

1049cdef cudaError_t _cudaDeviceRegisterAsyncNotification(int device, cudaAsyncCallback callbackFunc, void* userData, cudaAsyncCallbackHandle_t* callback) except ?cudaErrorCallRequiresNewerDriver nogil: 

1050 return _static_cudaDeviceRegisterAsyncNotification(device, callbackFunc, userData, callback) 

1051  

1052  

1053cdef cudaError_t _cudaDeviceUnregisterAsyncNotification(int device, cudaAsyncCallbackHandle_t callback) except ?cudaErrorCallRequiresNewerDriver nogil: 

1054 return _static_cudaDeviceUnregisterAsyncNotification(device, callback) 

1055  

1056  

1057cdef cudaError_t _cudaDeviceGetSharedMemConfig(cudaSharedMemConfig* pConfig) except ?cudaErrorCallRequiresNewerDriver nogil: 

1058 return _static_cudaDeviceGetSharedMemConfig(pConfig) 

1059  

1060  

1061cdef cudaError_t _cudaDeviceSetSharedMemConfig(cudaSharedMemConfig config) except ?cudaErrorCallRequiresNewerDriver nogil: 

1062 return _static_cudaDeviceSetSharedMemConfig(config) 

1063  

1064  

1065cdef cudaError_t _cudaGetLastError() except ?cudaErrorCallRequiresNewerDriver nogil: 

1066 return _static_cudaGetLastError() 

1067  

1068  

1069cdef cudaError_t _cudaPeekAtLastError() except ?cudaErrorCallRequiresNewerDriver nogil: 

1070 return _static_cudaPeekAtLastError() 

1071  

1072  

1073cdef const char* _cudaGetErrorName(cudaError_t error) except?NULL nogil: 

1074 return _static_cudaGetErrorName(error) 

1075  

1076  

1077cdef const char* _cudaGetErrorString(cudaError_t error) except?NULL nogil: 

1078 return _static_cudaGetErrorString(error) 

1079  

1080  

1081cdef cudaError_t _cudaGetDeviceCount(int* count) except ?cudaErrorCallRequiresNewerDriver nogil: 

1082 return _static_cudaGetDeviceCount(count) 

1083  

1084  

1085cdef cudaError_t _cudaDeviceGetAttribute(int* value, cudaDeviceAttr attr, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1086 return _static_cudaDeviceGetAttribute(value, attr, device) 

1087  

1088  

1089cdef cudaError_t _cudaDeviceGetDefaultMemPool(cudaMemPool_t* memPool, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1090 return _static_cudaDeviceGetDefaultMemPool(memPool, device) 

1091  

1092  

1093cdef cudaError_t _cudaDeviceSetMemPool(int device, cudaMemPool_t memPool) except ?cudaErrorCallRequiresNewerDriver nogil: 

1094 return _static_cudaDeviceSetMemPool(device, memPool) 

1095  

1096  

1097cdef cudaError_t _cudaDeviceGetMemPool(cudaMemPool_t* memPool, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1098 return _static_cudaDeviceGetMemPool(memPool, device) 

1099  

1100  

1101cdef cudaError_t _cudaDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, int device, int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1102 return _static_cudaDeviceGetNvSciSyncAttributes(nvSciSyncAttrList, device, flags) 

1103  

1104  

1105cdef cudaError_t _cudaDeviceGetP2PAttribute(int* value, cudaDeviceP2PAttr attr, int srcDevice, int dstDevice) except ?cudaErrorCallRequiresNewerDriver nogil: 

1106 return _static_cudaDeviceGetP2PAttribute(value, attr, srcDevice, dstDevice) 

1107  

1108  

1109cdef cudaError_t _cudaChooseDevice(int* device, const cudaDeviceProp* prop) except ?cudaErrorCallRequiresNewerDriver nogil: 

1110 return _static_cudaChooseDevice(device, prop) 

1111  

1112  

1113cdef cudaError_t _cudaInitDevice(int device, unsigned int deviceFlags, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1114 return _static_cudaInitDevice(device, deviceFlags, flags) 

1115  

1116  

1117cdef cudaError_t _cudaSetDevice(int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1118 return _static_cudaSetDevice(device) 

1119  

1120  

1121cdef cudaError_t _cudaGetDevice(int* device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1122 return _static_cudaGetDevice(device) 

1123  

1124  

1125cdef cudaError_t _cudaSetDeviceFlags(unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1126 return _static_cudaSetDeviceFlags(flags) 

1127  

1128  

1129cdef cudaError_t _cudaGetDeviceFlags(unsigned int* flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1130 return _static_cudaGetDeviceFlags(flags) 

1131  

1132  

1133cdef cudaError_t _cudaStreamCreate(cudaStream_t* pStream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1134 return _static_cudaStreamCreate(pStream) 

1135  

1136  

1137cdef cudaError_t _cudaStreamCreateWithFlags(cudaStream_t* pStream, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1138 return _static_cudaStreamCreateWithFlags(pStream, flags) 

1139  

1140  

1141cdef cudaError_t _cudaStreamCreateWithPriority(cudaStream_t* pStream, unsigned int flags, int priority) except ?cudaErrorCallRequiresNewerDriver nogil: 

1142 return _static_cudaStreamCreateWithPriority(pStream, flags, priority) 

1143  

1144  

1145cdef cudaError_t _cudaStreamGetPriority(cudaStream_t hStream, int* priority) except ?cudaErrorCallRequiresNewerDriver nogil: 

1146 return _static_cudaStreamGetPriority(hStream, priority) 

1147  

1148  

1149cdef cudaError_t _cudaStreamGetFlags(cudaStream_t hStream, unsigned int* flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1150 return _static_cudaStreamGetFlags(hStream, flags) 

1151  

1152  

1153cdef cudaError_t _cudaStreamGetId(cudaStream_t hStream, unsigned long long* streamId) except ?cudaErrorCallRequiresNewerDriver nogil: 

1154 return _static_cudaStreamGetId(hStream, streamId) 

1155  

1156  

1157cdef cudaError_t _cudaStreamGetDevice(cudaStream_t hStream, int* device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1158 return _static_cudaStreamGetDevice(hStream, device) 

1159  

1160  

1161cdef cudaError_t _cudaCtxResetPersistingL2Cache() except ?cudaErrorCallRequiresNewerDriver nogil: 

1162 return _static_cudaCtxResetPersistingL2Cache() 

1163  

1164  

1165cdef cudaError_t _cudaStreamCopyAttributes(cudaStream_t dst, cudaStream_t src) except ?cudaErrorCallRequiresNewerDriver nogil: 

1166 return _static_cudaStreamCopyAttributes(dst, src) 

1167  

1168  

1169cdef cudaError_t _cudaStreamGetAttribute(cudaStream_t hStream, cudaStreamAttrID attr, cudaStreamAttrValue* value_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

1170 return _static_cudaStreamGetAttribute(hStream, attr, value_out) 

1171  

1172  

1173cdef cudaError_t _cudaStreamSetAttribute(cudaStream_t hStream, cudaStreamAttrID attr, const cudaStreamAttrValue* value) except ?cudaErrorCallRequiresNewerDriver nogil: 

1174 return _static_cudaStreamSetAttribute(hStream, attr, value) 

1175  

1176  

1177cdef cudaError_t _cudaStreamDestroy(cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1178 return _static_cudaStreamDestroy(stream) 

1179  

1180  

1181cdef cudaError_t _cudaStreamWaitEvent(cudaStream_t stream, cudaEvent_t event, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1182 return _static_cudaStreamWaitEvent(stream, event, flags) 

1183  

1184  

1185cdef cudaError_t _cudaStreamAddCallback(cudaStream_t stream, cudaStreamCallback_t callback, void* userData, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1186 return _static_cudaStreamAddCallback(stream, callback, userData, flags) 

1187  

1188  

1189cdef cudaError_t _cudaStreamSynchronize(cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1190 return _static_cudaStreamSynchronize(stream) 

1191  

1192  

1193cdef cudaError_t _cudaStreamQuery(cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1194 return _static_cudaStreamQuery(stream) 

1195  

1196  

1197cdef cudaError_t _cudaStreamAttachMemAsync(cudaStream_t stream, void* devPtr, size_t length, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1198 return _static_cudaStreamAttachMemAsync(stream, devPtr, length, flags) 

1199  

1200  

1201cdef cudaError_t _cudaStreamBeginCapture(cudaStream_t stream, cudaStreamCaptureMode mode) except ?cudaErrorCallRequiresNewerDriver nogil: 

1202 return _static_cudaStreamBeginCapture(stream, mode) 

1203  

1204  

1205cdef cudaError_t _cudaStreamBeginCaptureToGraph(cudaStream_t stream, cudaGraph_t graph, const cudaGraphNode_t* dependencies, const cudaGraphEdgeData* dependencyData, size_t numDependencies, cudaStreamCaptureMode mode) except ?cudaErrorCallRequiresNewerDriver nogil: 

1206 return _static_cudaStreamBeginCaptureToGraph(stream, graph, dependencies, dependencyData, numDependencies, mode) 

1207  

1208  

1209cdef cudaError_t _cudaThreadExchangeStreamCaptureMode(cudaStreamCaptureMode* mode) except ?cudaErrorCallRequiresNewerDriver nogil: 

1210 return _static_cudaThreadExchangeStreamCaptureMode(mode) 

1211  

1212  

1213cdef cudaError_t _cudaStreamEndCapture(cudaStream_t stream, cudaGraph_t* pGraph) except ?cudaErrorCallRequiresNewerDriver nogil: 

1214 return _static_cudaStreamEndCapture(stream, pGraph) 

1215  

1216  

1217cdef cudaError_t _cudaStreamIsCapturing(cudaStream_t stream, cudaStreamCaptureStatus* pCaptureStatus) except ?cudaErrorCallRequiresNewerDriver nogil: 

1218 return _static_cudaStreamIsCapturing(stream, pCaptureStatus) 

1219  

1220  

1221cdef cudaError_t _cudaStreamUpdateCaptureDependencies(cudaStream_t stream, cudaGraphNode_t* dependencies, const cudaGraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1222 return _static_cudaStreamUpdateCaptureDependencies(stream, dependencies, dependencyData, numDependencies, flags) 

1223  

1224  

1225cdef cudaError_t _cudaEventCreate(cudaEvent_t* event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1226 return _static_cudaEventCreate(event) 

1227  

1228  

1229cdef cudaError_t _cudaEventCreateWithFlags(cudaEvent_t* event, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1230 return _static_cudaEventCreateWithFlags(event, flags) 

1231  

1232  

1233cdef cudaError_t _cudaEventRecord(cudaEvent_t event, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1234 return _static_cudaEventRecord(event, stream) 

1235  

1236  

1237cdef cudaError_t _cudaEventRecordWithFlags(cudaEvent_t event, cudaStream_t stream, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1238 return _static_cudaEventRecordWithFlags(event, stream, flags) 

1239  

1240  

1241cdef cudaError_t _cudaEventQuery(cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1242 return _static_cudaEventQuery(event) 

1243  

1244  

1245cdef cudaError_t _cudaEventSynchronize(cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1246 return _static_cudaEventSynchronize(event) 

1247  

1248  

1249cdef cudaError_t _cudaEventDestroy(cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1250 return _static_cudaEventDestroy(event) 

1251  

1252  

1253cdef cudaError_t _cudaEventElapsedTime(float* ms, cudaEvent_t start, cudaEvent_t end) except ?cudaErrorCallRequiresNewerDriver nogil: 

1254 return _static_cudaEventElapsedTime(ms, start, end) 

1255  

1256  

1257cdef cudaError_t _cudaImportExternalMemory(cudaExternalMemory_t* extMem_out, const cudaExternalMemoryHandleDesc* memHandleDesc) except ?cudaErrorCallRequiresNewerDriver nogil: 

1258 return _static_cudaImportExternalMemory(extMem_out, memHandleDesc) 

1259  

1260  

1261cdef cudaError_t _cudaExternalMemoryGetMappedBuffer(void** devPtr, cudaExternalMemory_t extMem, const cudaExternalMemoryBufferDesc* bufferDesc) except ?cudaErrorCallRequiresNewerDriver nogil: 

1262 return _static_cudaExternalMemoryGetMappedBuffer(devPtr, extMem, bufferDesc) 

1263  

1264  

1265cdef cudaError_t _cudaExternalMemoryGetMappedMipmappedArray(cudaMipmappedArray_t* mipmap, cudaExternalMemory_t extMem, const cudaExternalMemoryMipmappedArrayDesc* mipmapDesc) except ?cudaErrorCallRequiresNewerDriver nogil: 

1266 return _static_cudaExternalMemoryGetMappedMipmappedArray(mipmap, extMem, mipmapDesc) 

1267  

1268  

1269cdef cudaError_t _cudaDestroyExternalMemory(cudaExternalMemory_t extMem) except ?cudaErrorCallRequiresNewerDriver nogil: 

1270 return _static_cudaDestroyExternalMemory(extMem) 

1271  

1272  

1273cdef cudaError_t _cudaImportExternalSemaphore(cudaExternalSemaphore_t* extSem_out, const cudaExternalSemaphoreHandleDesc* semHandleDesc) except ?cudaErrorCallRequiresNewerDriver nogil: 

1274 return _static_cudaImportExternalSemaphore(extSem_out, semHandleDesc) 

1275  

1276  

1277cdef cudaError_t _cudaDestroyExternalSemaphore(cudaExternalSemaphore_t extSem) except ?cudaErrorCallRequiresNewerDriver nogil: 

1278 return _static_cudaDestroyExternalSemaphore(extSem) 

1279  

1280  

1281cdef cudaError_t _cudaFuncSetCacheConfig(const void* func, cudaFuncCache cacheConfig) except ?cudaErrorCallRequiresNewerDriver nogil: 

1282 return _static_cudaFuncSetCacheConfig(func, cacheConfig) 

1283  

1284  

1285cdef cudaError_t _cudaFuncGetAttributes(cudaFuncAttributes* attr, const void* func) except ?cudaErrorCallRequiresNewerDriver nogil: 

1286 return _static_cudaFuncGetAttributes(attr, func) 

1287  

1288  

1289cdef cudaError_t _cudaFuncSetAttribute(const void* func, cudaFuncAttribute attr, int value) except ?cudaErrorCallRequiresNewerDriver nogil: 

1290 return _static_cudaFuncSetAttribute(func, attr, value) 

1291  

1292  

1293cdef cudaError_t _cudaFuncGetName(const char** name, const void* func) except ?cudaErrorCallRequiresNewerDriver nogil: 

1294 return _static_cudaFuncGetName(name, func) 

1295  

1296  

1297cdef cudaError_t _cudaFuncGetParamInfo(const void* func, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?cudaErrorCallRequiresNewerDriver nogil: 

1298 return _static_cudaFuncGetParamInfo(func, paramIndex, paramOffset, paramSize) 

1299  

1300  

1301cdef cudaError_t _cudaLaunchHostFunc(cudaStream_t stream, cudaHostFn_t fn, void* userData) except ?cudaErrorCallRequiresNewerDriver nogil: 

1302 return _static_cudaLaunchHostFunc(stream, fn, userData) 

1303  

1304  

1305cdef cudaError_t _cudaFuncSetSharedMemConfig(const void* func, cudaSharedMemConfig config) except ?cudaErrorCallRequiresNewerDriver nogil: 

1306 return _static_cudaFuncSetSharedMemConfig(func, config) 

1307  

1308  

1309cdef cudaError_t _cudaOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, const void* func, int blockSize, size_t dynamicSMemSize) except ?cudaErrorCallRequiresNewerDriver nogil: 

1310 return _static_cudaOccupancyMaxActiveBlocksPerMultiprocessor(numBlocks, func, blockSize, dynamicSMemSize) 

1311  

1312  

1313cdef cudaError_t _cudaOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, const void* func, int numBlocks, int blockSize) except ?cudaErrorCallRequiresNewerDriver nogil: 

1314 return _static_cudaOccupancyAvailableDynamicSMemPerBlock(dynamicSmemSize, func, numBlocks, blockSize) 

1315  

1316  

1317cdef cudaError_t _cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int* numBlocks, const void* func, int blockSize, size_t dynamicSMemSize, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1318 return _static_cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(numBlocks, func, blockSize, dynamicSMemSize, flags) 

1319  

1320  

1321cdef cudaError_t _cudaMallocManaged(void** devPtr, size_t size, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1322 return _static_cudaMallocManaged(devPtr, size, flags) 

1323  

1324  

1325cdef cudaError_t _cudaMalloc(void** devPtr, size_t size) except ?cudaErrorCallRequiresNewerDriver nogil: 

1326 return _static_cudaMalloc(devPtr, size) 

1327  

1328  

1329cdef cudaError_t _cudaMallocHost(void** ptr, size_t size) except ?cudaErrorCallRequiresNewerDriver nogil: 

1330 return _static_cudaMallocHost(ptr, size) 

1331  

1332  

1333cdef cudaError_t _cudaMallocPitch(void** devPtr, size_t* pitch, size_t width, size_t height) except ?cudaErrorCallRequiresNewerDriver nogil: 

1334 return _static_cudaMallocPitch(devPtr, pitch, width, height) 

1335  

1336  

1337cdef cudaError_t _cudaMallocArray(cudaArray_t* array, const cudaChannelFormatDesc* desc, size_t width, size_t height, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1338 return _static_cudaMallocArray(array, desc, width, height, flags) 

1339  

1340  

1341cdef cudaError_t _cudaFree(void* devPtr) except ?cudaErrorCallRequiresNewerDriver nogil: 

1342 return _static_cudaFree(devPtr) 

1343  

1344  

1345cdef cudaError_t _cudaFreeHost(void* ptr) except ?cudaErrorCallRequiresNewerDriver nogil: 

1346 return _static_cudaFreeHost(ptr) 

1347  

1348  

1349cdef cudaError_t _cudaFreeArray(cudaArray_t array) except ?cudaErrorCallRequiresNewerDriver nogil: 

1350 return _static_cudaFreeArray(array) 

1351  

1352  

1353cdef cudaError_t _cudaFreeMipmappedArray(cudaMipmappedArray_t mipmappedArray) except ?cudaErrorCallRequiresNewerDriver nogil: 

1354 return _static_cudaFreeMipmappedArray(mipmappedArray) 

1355  

1356  

1357cdef cudaError_t _cudaHostAlloc(void** pHost, size_t size, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1358 return _static_cudaHostAlloc(pHost, size, flags) 

1359  

1360  

1361cdef cudaError_t _cudaHostRegister(void* ptr, size_t size, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1362 return _static_cudaHostRegister(ptr, size, flags) 

1363  

1364  

1365cdef cudaError_t _cudaHostUnregister(void* ptr) except ?cudaErrorCallRequiresNewerDriver nogil: 

1366 return _static_cudaHostUnregister(ptr) 

1367  

1368  

1369cdef cudaError_t _cudaHostGetDevicePointer(void** pDevice, void* pHost, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1370 return _static_cudaHostGetDevicePointer(pDevice, pHost, flags) 

1371  

1372  

1373cdef cudaError_t _cudaHostGetFlags(unsigned int* pFlags, void* pHost) except ?cudaErrorCallRequiresNewerDriver nogil: 

1374 return _static_cudaHostGetFlags(pFlags, pHost) 

1375  

1376  

1377cdef cudaError_t _cudaMalloc3D(cudaPitchedPtr* pitchedDevPtr, cudaExtent extent) except ?cudaErrorCallRequiresNewerDriver nogil: 

1378 return _static_cudaMalloc3D(pitchedDevPtr, extent) 

1379  

1380  

1381cdef cudaError_t _cudaMalloc3DArray(cudaArray_t* array, const cudaChannelFormatDesc* desc, cudaExtent extent, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1382 return _static_cudaMalloc3DArray(array, desc, extent, flags) 

1383  

1384  

1385cdef cudaError_t _cudaMallocMipmappedArray(cudaMipmappedArray_t* mipmappedArray, const cudaChannelFormatDesc* desc, cudaExtent extent, unsigned int numLevels, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1386 return _static_cudaMallocMipmappedArray(mipmappedArray, desc, extent, numLevels, flags) 

1387  

1388  

1389cdef cudaError_t _cudaGetMipmappedArrayLevel(cudaArray_t* levelArray, cudaMipmappedArray_const_t mipmappedArray, unsigned int level) except ?cudaErrorCallRequiresNewerDriver nogil: 

1390 return _static_cudaGetMipmappedArrayLevel(levelArray, mipmappedArray, level) 

1391  

1392  

1393cdef cudaError_t _cudaMemcpy3D(const cudaMemcpy3DParms* p) except ?cudaErrorCallRequiresNewerDriver nogil: 

1394 return _static_cudaMemcpy3D(p) 

1395  

1396  

1397cdef cudaError_t _cudaMemcpy3DPeer(const cudaMemcpy3DPeerParms* p) except ?cudaErrorCallRequiresNewerDriver nogil: 

1398 return _static_cudaMemcpy3DPeer(p) 

1399  

1400  

1401cdef cudaError_t _cudaMemcpy3DAsync(const cudaMemcpy3DParms* p, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1402 return _static_cudaMemcpy3DAsync(p, stream) 

1403  

1404  

1405cdef cudaError_t _cudaMemcpy3DPeerAsync(const cudaMemcpy3DPeerParms* p, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1406 return _static_cudaMemcpy3DPeerAsync(p, stream) 

1407  

1408  

1409cdef cudaError_t _cudaMemGetInfo(size_t* free, size_t* total) except ?cudaErrorCallRequiresNewerDriver nogil: 

1410 return _static_cudaMemGetInfo(free, total) 

1411  

1412  

1413cdef cudaError_t _cudaArrayGetInfo(cudaChannelFormatDesc* desc, cudaExtent* extent, unsigned int* flags, cudaArray_t array) except ?cudaErrorCallRequiresNewerDriver nogil: 

1414 return _static_cudaArrayGetInfo(desc, extent, flags, array) 

1415  

1416  

1417cdef cudaError_t _cudaArrayGetPlane(cudaArray_t* pPlaneArray, cudaArray_t hArray, unsigned int planeIdx) except ?cudaErrorCallRequiresNewerDriver nogil: 

1418 return _static_cudaArrayGetPlane(pPlaneArray, hArray, planeIdx) 

1419  

1420  

1421cdef cudaError_t _cudaArrayGetMemoryRequirements(cudaArrayMemoryRequirements* memoryRequirements, cudaArray_t array, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1422 return _static_cudaArrayGetMemoryRequirements(memoryRequirements, array, device) 

1423  

1424  

1425cdef cudaError_t _cudaMipmappedArrayGetMemoryRequirements(cudaArrayMemoryRequirements* memoryRequirements, cudaMipmappedArray_t mipmap, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1426 return _static_cudaMipmappedArrayGetMemoryRequirements(memoryRequirements, mipmap, device) 

1427  

1428  

1429cdef cudaError_t _cudaArrayGetSparseProperties(cudaArraySparseProperties* sparseProperties, cudaArray_t array) except ?cudaErrorCallRequiresNewerDriver nogil: 

1430 return _static_cudaArrayGetSparseProperties(sparseProperties, array) 

1431  

1432  

1433cdef cudaError_t _cudaMipmappedArrayGetSparseProperties(cudaArraySparseProperties* sparseProperties, cudaMipmappedArray_t mipmap) except ?cudaErrorCallRequiresNewerDriver nogil: 

1434 return _static_cudaMipmappedArrayGetSparseProperties(sparseProperties, mipmap) 

1435  

1436  

1437cdef cudaError_t _cudaMemcpy(void* dst, const void* src, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1438 return _static_cudaMemcpy(dst, src, count, kind) 

1439  

1440  

1441cdef cudaError_t _cudaMemcpyPeer(void* dst, int dstDevice, const void* src, int srcDevice, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil: 

1442 return _static_cudaMemcpyPeer(dst, dstDevice, src, srcDevice, count) 

1443  

1444  

1445cdef cudaError_t _cudaMemcpy2D(void* dst, size_t dpitch, const void* src, size_t spitch, size_t width, size_t height, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1446 return _static_cudaMemcpy2D(dst, dpitch, src, spitch, width, height, kind) 

1447  

1448  

1449cdef cudaError_t _cudaMemcpy2DToArray(cudaArray_t dst, size_t wOffset, size_t hOffset, const void* src, size_t spitch, size_t width, size_t height, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1450 return _static_cudaMemcpy2DToArray(dst, wOffset, hOffset, src, spitch, width, height, kind) 

1451  

1452  

1453cdef cudaError_t _cudaMemcpy2DFromArray(void* dst, size_t dpitch, cudaArray_const_t src, size_t wOffset, size_t hOffset, size_t width, size_t height, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1454 return _static_cudaMemcpy2DFromArray(dst, dpitch, src, wOffset, hOffset, width, height, kind) 

1455  

1456  

1457cdef cudaError_t _cudaMemcpy2DArrayToArray(cudaArray_t dst, size_t wOffsetDst, size_t hOffsetDst, cudaArray_const_t src, size_t wOffsetSrc, size_t hOffsetSrc, size_t width, size_t height, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1458 return _static_cudaMemcpy2DArrayToArray(dst, wOffsetDst, hOffsetDst, src, wOffsetSrc, hOffsetSrc, width, height, kind) 

1459  

1460  

1461cdef cudaError_t _cudaMemcpyAsync(void* dst, const void* src, size_t count, cudaMemcpyKind kind, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1462 return _static_cudaMemcpyAsync(dst, src, count, kind, stream) 

1463  

1464  

1465cdef cudaError_t _cudaMemcpyPeerAsync(void* dst, int dstDevice, const void* src, int srcDevice, size_t count, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1466 return _static_cudaMemcpyPeerAsync(dst, dstDevice, src, srcDevice, count, stream) 

1467  

1468  

1469cdef cudaError_t _cudaMemcpyBatchAsync(const void** dsts, const void** srcs, const size_t* sizes, size_t count, cudaMemcpyAttributes* attrs, size_t* attrsIdxs, size_t numAttrs, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1470 return _static_cudaMemcpyBatchAsync(dsts, srcs, sizes, count, attrs, attrsIdxs, numAttrs, stream) 

1471  

1472  

1473cdef cudaError_t _cudaMemcpy3DBatchAsync(size_t numOps, cudaMemcpy3DBatchOp* opList, unsigned long long flags, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1474 return _static_cudaMemcpy3DBatchAsync(numOps, opList, flags, stream) 

1475  

1476  

1477cdef cudaError_t _cudaMemcpy2DAsync(void* dst, size_t dpitch, const void* src, size_t spitch, size_t width, size_t height, cudaMemcpyKind kind, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1478 return _static_cudaMemcpy2DAsync(dst, dpitch, src, spitch, width, height, kind, stream) 

1479  

1480  

1481cdef cudaError_t _cudaMemcpy2DToArrayAsync(cudaArray_t dst, size_t wOffset, size_t hOffset, const void* src, size_t spitch, size_t width, size_t height, cudaMemcpyKind kind, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1482 return _static_cudaMemcpy2DToArrayAsync(dst, wOffset, hOffset, src, spitch, width, height, kind, stream) 

1483  

1484  

1485cdef cudaError_t _cudaMemcpy2DFromArrayAsync(void* dst, size_t dpitch, cudaArray_const_t src, size_t wOffset, size_t hOffset, size_t width, size_t height, cudaMemcpyKind kind, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1486 return _static_cudaMemcpy2DFromArrayAsync(dst, dpitch, src, wOffset, hOffset, width, height, kind, stream) 

1487  

1488  

1489cdef cudaError_t _cudaMemset(void* devPtr, int value, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil: 

1490 return _static_cudaMemset(devPtr, value, count) 

1491  

1492  

1493cdef cudaError_t _cudaMemset2D(void* devPtr, size_t pitch, int value, size_t width, size_t height) except ?cudaErrorCallRequiresNewerDriver nogil: 

1494 return _static_cudaMemset2D(devPtr, pitch, value, width, height) 

1495  

1496  

1497cdef cudaError_t _cudaMemset3D(cudaPitchedPtr pitchedDevPtr, int value, cudaExtent extent) except ?cudaErrorCallRequiresNewerDriver nogil: 

1498 return _static_cudaMemset3D(pitchedDevPtr, value, extent) 

1499  

1500  

1501cdef cudaError_t _cudaMemsetAsync(void* devPtr, int value, size_t count, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1502 return _static_cudaMemsetAsync(devPtr, value, count, stream) 

1503  

1504  

1505cdef cudaError_t _cudaMemset2DAsync(void* devPtr, size_t pitch, int value, size_t width, size_t height, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1506 return _static_cudaMemset2DAsync(devPtr, pitch, value, width, height, stream) 

1507  

1508  

1509cdef cudaError_t _cudaMemset3DAsync(cudaPitchedPtr pitchedDevPtr, int value, cudaExtent extent, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1510 return _static_cudaMemset3DAsync(pitchedDevPtr, value, extent, stream) 

1511  

1512  

1513cdef cudaError_t _cudaMemPrefetchAsync(const void* devPtr, size_t count, cudaMemLocation location, unsigned int flags, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1514 return _static_cudaMemPrefetchAsync(devPtr, count, location, flags, stream) 

1515  

1516  

1517cdef cudaError_t _cudaMemAdvise(const void* devPtr, size_t count, cudaMemoryAdvise advice, cudaMemLocation location) except ?cudaErrorCallRequiresNewerDriver nogil: 

1518 return _static_cudaMemAdvise(devPtr, count, advice, location) 

1519  

1520  

1521cdef cudaError_t _cudaMemRangeGetAttribute(void* data, size_t dataSize, cudaMemRangeAttribute attribute, const void* devPtr, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil: 

1522 return _static_cudaMemRangeGetAttribute(data, dataSize, attribute, devPtr, count) 

1523  

1524  

1525cdef cudaError_t _cudaMemRangeGetAttributes(void** data, size_t* dataSizes, cudaMemRangeAttribute* attributes, size_t numAttributes, const void* devPtr, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil: 

1526 return _static_cudaMemRangeGetAttributes(data, dataSizes, attributes, numAttributes, devPtr, count) 

1527  

1528  

1529cdef cudaError_t _cudaMemcpyToArray(cudaArray_t dst, size_t wOffset, size_t hOffset, const void* src, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1530 return _static_cudaMemcpyToArray(dst, wOffset, hOffset, src, count, kind) 

1531  

1532  

1533cdef cudaError_t _cudaMemcpyFromArray(void* dst, cudaArray_const_t src, size_t wOffset, size_t hOffset, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1534 return _static_cudaMemcpyFromArray(dst, src, wOffset, hOffset, count, kind) 

1535  

1536  

1537cdef cudaError_t _cudaMemcpyArrayToArray(cudaArray_t dst, size_t wOffsetDst, size_t hOffsetDst, cudaArray_const_t src, size_t wOffsetSrc, size_t hOffsetSrc, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1538 return _static_cudaMemcpyArrayToArray(dst, wOffsetDst, hOffsetDst, src, wOffsetSrc, hOffsetSrc, count, kind) 

1539  

1540  

1541cdef cudaError_t _cudaMemcpyToArrayAsync(cudaArray_t dst, size_t wOffset, size_t hOffset, const void* src, size_t count, cudaMemcpyKind kind, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1542 return _static_cudaMemcpyToArrayAsync(dst, wOffset, hOffset, src, count, kind, stream) 

1543  

1544  

1545cdef cudaError_t _cudaMemcpyFromArrayAsync(void* dst, cudaArray_const_t src, size_t wOffset, size_t hOffset, size_t count, cudaMemcpyKind kind, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1546 return _static_cudaMemcpyFromArrayAsync(dst, src, wOffset, hOffset, count, kind, stream) 

1547  

1548  

1549cdef cudaError_t _cudaMallocAsync(void** devPtr, size_t size, cudaStream_t hStream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1550 return _static_cudaMallocAsync(devPtr, size, hStream) 

1551  

1552  

1553cdef cudaError_t _cudaFreeAsync(void* devPtr, cudaStream_t hStream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1554 return _static_cudaFreeAsync(devPtr, hStream) 

1555  

1556  

1557cdef cudaError_t _cudaMemPoolTrimTo(cudaMemPool_t memPool, size_t minBytesToKeep) except ?cudaErrorCallRequiresNewerDriver nogil: 

1558 return _static_cudaMemPoolTrimTo(memPool, minBytesToKeep) 

1559  

1560  

1561cdef cudaError_t _cudaMemPoolSetAttribute(cudaMemPool_t memPool, cudaMemPoolAttr attr, void* value) except ?cudaErrorCallRequiresNewerDriver nogil: 

1562 return _static_cudaMemPoolSetAttribute(memPool, attr, value) 

1563  

1564  

1565cdef cudaError_t _cudaMemPoolGetAttribute(cudaMemPool_t memPool, cudaMemPoolAttr attr, void* value) except ?cudaErrorCallRequiresNewerDriver nogil: 

1566 return _static_cudaMemPoolGetAttribute(memPool, attr, value) 

1567  

1568  

1569cdef cudaError_t _cudaMemPoolSetAccess(cudaMemPool_t memPool, const cudaMemAccessDesc* descList, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil: 

1570 return _static_cudaMemPoolSetAccess(memPool, descList, count) 

1571  

1572  

1573cdef cudaError_t _cudaMemPoolGetAccess(cudaMemAccessFlags* flags, cudaMemPool_t memPool, cudaMemLocation* location) except ?cudaErrorCallRequiresNewerDriver nogil: 

1574 return _static_cudaMemPoolGetAccess(flags, memPool, location) 

1575  

1576  

1577cdef cudaError_t _cudaMemPoolCreate(cudaMemPool_t* memPool, const cudaMemPoolProps* poolProps) except ?cudaErrorCallRequiresNewerDriver nogil: 

1578 return _static_cudaMemPoolCreate(memPool, poolProps) 

1579  

1580  

1581cdef cudaError_t _cudaMemPoolDestroy(cudaMemPool_t memPool) except ?cudaErrorCallRequiresNewerDriver nogil: 

1582 return _static_cudaMemPoolDestroy(memPool) 

1583  

1584  

1585cdef cudaError_t _cudaMallocFromPoolAsync(void** ptr, size_t size, cudaMemPool_t memPool, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1586 return _static_cudaMallocFromPoolAsync(ptr, size, memPool, stream) 

1587  

1588  

1589cdef cudaError_t _cudaMemPoolExportToShareableHandle(void* shareableHandle, cudaMemPool_t memPool, cudaMemAllocationHandleType handleType, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1590 return _static_cudaMemPoolExportToShareableHandle(shareableHandle, memPool, handleType, flags) 

1591  

1592  

1593cdef cudaError_t _cudaMemPoolImportFromShareableHandle(cudaMemPool_t* memPool, void* shareableHandle, cudaMemAllocationHandleType handleType, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1594 return _static_cudaMemPoolImportFromShareableHandle(memPool, shareableHandle, handleType, flags) 

1595  

1596  

1597cdef cudaError_t _cudaMemPoolExportPointer(cudaMemPoolPtrExportData* exportData, void* ptr) except ?cudaErrorCallRequiresNewerDriver nogil: 

1598 return _static_cudaMemPoolExportPointer(exportData, ptr) 

1599  

1600  

1601cdef cudaError_t _cudaMemPoolImportPointer(void** ptr, cudaMemPool_t memPool, cudaMemPoolPtrExportData* exportData) except ?cudaErrorCallRequiresNewerDriver nogil: 

1602 return _static_cudaMemPoolImportPointer(ptr, memPool, exportData) 

1603  

1604  

1605cdef cudaError_t _cudaPointerGetAttributes(cudaPointerAttributes* attributes, const void* ptr) except ?cudaErrorCallRequiresNewerDriver nogil: 

1606 return _static_cudaPointerGetAttributes(attributes, ptr) 

1607  

1608  

1609cdef cudaError_t _cudaDeviceCanAccessPeer(int* canAccessPeer, int device, int peerDevice) except ?cudaErrorCallRequiresNewerDriver nogil: 

1610 return _static_cudaDeviceCanAccessPeer(canAccessPeer, device, peerDevice) 

1611  

1612  

1613cdef cudaError_t _cudaDeviceEnablePeerAccess(int peerDevice, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1614 return _static_cudaDeviceEnablePeerAccess(peerDevice, flags) 

1615  

1616  

1617cdef cudaError_t _cudaDeviceDisablePeerAccess(int peerDevice) except ?cudaErrorCallRequiresNewerDriver nogil: 

1618 return _static_cudaDeviceDisablePeerAccess(peerDevice) 

1619  

1620  

1621cdef cudaError_t _cudaGraphicsUnregisterResource(cudaGraphicsResource_t resource) except ?cudaErrorCallRequiresNewerDriver nogil: 

1622 return _static_cudaGraphicsUnregisterResource(resource) 

1623  

1624  

1625cdef cudaError_t _cudaGraphicsResourceSetMapFlags(cudaGraphicsResource_t resource, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1626 return _static_cudaGraphicsResourceSetMapFlags(resource, flags) 

1627  

1628  

1629cdef cudaError_t _cudaGraphicsMapResources(int count, cudaGraphicsResource_t* resources, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1630 return _static_cudaGraphicsMapResources(count, resources, stream) 

1631  

1632  

1633cdef cudaError_t _cudaGraphicsUnmapResources(int count, cudaGraphicsResource_t* resources, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1634 return _static_cudaGraphicsUnmapResources(count, resources, stream) 

1635  

1636  

1637cdef cudaError_t _cudaGraphicsResourceGetMappedPointer(void** devPtr, size_t* size, cudaGraphicsResource_t resource) except ?cudaErrorCallRequiresNewerDriver nogil: 

1638 return _static_cudaGraphicsResourceGetMappedPointer(devPtr, size, resource) 

1639  

1640  

1641cdef cudaError_t _cudaGraphicsSubResourceGetMappedArray(cudaArray_t* array, cudaGraphicsResource_t resource, unsigned int arrayIndex, unsigned int mipLevel) except ?cudaErrorCallRequiresNewerDriver nogil: 

1642 return _static_cudaGraphicsSubResourceGetMappedArray(array, resource, arrayIndex, mipLevel) 

1643  

1644  

1645cdef cudaError_t _cudaGraphicsResourceGetMappedMipmappedArray(cudaMipmappedArray_t* mipmappedArray, cudaGraphicsResource_t resource) except ?cudaErrorCallRequiresNewerDriver nogil: 

1646 return _static_cudaGraphicsResourceGetMappedMipmappedArray(mipmappedArray, resource) 

1647  

1648  

1649cdef cudaError_t _cudaGetChannelDesc(cudaChannelFormatDesc* desc, cudaArray_const_t array) except ?cudaErrorCallRequiresNewerDriver nogil: 

1650 return _static_cudaGetChannelDesc(desc, array) 

1651  

1652  

1653cdef cudaChannelFormatDesc _cudaCreateChannelDesc(int x, int y, int z, int w, cudaChannelFormatKind f) except* nogil: 

1654 return _static_cudaCreateChannelDesc(x, y, z, w, f) 

1655  

1656  

1657cdef cudaError_t _cudaCreateTextureObject(cudaTextureObject_t* pTexObject, const cudaResourceDesc* pResDesc, const cudaTextureDesc* pTexDesc, const cudaResourceViewDesc* pResViewDesc) except ?cudaErrorCallRequiresNewerDriver nogil: 

1658 return _static_cudaCreateTextureObject(pTexObject, pResDesc, pTexDesc, pResViewDesc) 

1659  

1660  

1661cdef cudaError_t _cudaDestroyTextureObject(cudaTextureObject_t texObject) except ?cudaErrorCallRequiresNewerDriver nogil: 

1662 return _static_cudaDestroyTextureObject(texObject) 

1663  

1664  

1665cdef cudaError_t _cudaGetTextureObjectResourceDesc(cudaResourceDesc* pResDesc, cudaTextureObject_t texObject) except ?cudaErrorCallRequiresNewerDriver nogil: 

1666 return _static_cudaGetTextureObjectResourceDesc(pResDesc, texObject) 

1667  

1668  

1669cdef cudaError_t _cudaGetTextureObjectTextureDesc(cudaTextureDesc* pTexDesc, cudaTextureObject_t texObject) except ?cudaErrorCallRequiresNewerDriver nogil: 

1670 return _static_cudaGetTextureObjectTextureDesc(pTexDesc, texObject) 

1671  

1672  

1673cdef cudaError_t _cudaGetTextureObjectResourceViewDesc(cudaResourceViewDesc* pResViewDesc, cudaTextureObject_t texObject) except ?cudaErrorCallRequiresNewerDriver nogil: 

1674 return _static_cudaGetTextureObjectResourceViewDesc(pResViewDesc, texObject) 

1675  

1676  

1677cdef cudaError_t _cudaCreateSurfaceObject(cudaSurfaceObject_t* pSurfObject, const cudaResourceDesc* pResDesc) except ?cudaErrorCallRequiresNewerDriver nogil: 

1678 return _static_cudaCreateSurfaceObject(pSurfObject, pResDesc) 

1679  

1680  

1681cdef cudaError_t _cudaDestroySurfaceObject(cudaSurfaceObject_t surfObject) except ?cudaErrorCallRequiresNewerDriver nogil: 

1682 return _static_cudaDestroySurfaceObject(surfObject) 

1683  

1684  

1685cdef cudaError_t _cudaGetSurfaceObjectResourceDesc(cudaResourceDesc* pResDesc, cudaSurfaceObject_t surfObject) except ?cudaErrorCallRequiresNewerDriver nogil: 

1686 return _static_cudaGetSurfaceObjectResourceDesc(pResDesc, surfObject) 

1687  

1688  

1689cdef cudaError_t _cudaDriverGetVersion(int* driverVersion) except ?cudaErrorCallRequiresNewerDriver nogil: 

1690 return _static_cudaDriverGetVersion(driverVersion) 

1691  

1692  

1693cdef cudaError_t _cudaRuntimeGetVersion(int* runtimeVersion) except ?cudaErrorCallRequiresNewerDriver nogil: 

1694 return _static_cudaRuntimeGetVersion(runtimeVersion) 

1695  

1696  

1697cdef cudaError_t _cudaGraphCreate(cudaGraph_t* pGraph, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1698 return _static_cudaGraphCreate(pGraph, flags) 

1699  

1700  

1701cdef cudaError_t _cudaGraphAddKernelNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaKernelNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1702 return _static_cudaGraphAddKernelNode(pGraphNode, graph, pDependencies, numDependencies, pNodeParams) 

1703  

1704  

1705cdef cudaError_t _cudaGraphKernelNodeGetParams(cudaGraphNode_t node, cudaKernelNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1706 return _static_cudaGraphKernelNodeGetParams(node, pNodeParams) 

1707  

1708  

1709cdef cudaError_t _cudaGraphKernelNodeSetParams(cudaGraphNode_t node, const cudaKernelNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1710 return _static_cudaGraphKernelNodeSetParams(node, pNodeParams) 

1711  

1712  

1713cdef cudaError_t _cudaGraphKernelNodeCopyAttributes(cudaGraphNode_t hDst, cudaGraphNode_t hSrc) except ?cudaErrorCallRequiresNewerDriver nogil: 

1714 return _static_cudaGraphKernelNodeCopyAttributes(hDst, hSrc) 

1715  

1716  

1717cdef cudaError_t _cudaGraphKernelNodeGetAttribute(cudaGraphNode_t hNode, cudaKernelNodeAttrID attr, cudaKernelNodeAttrValue* value_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

1718 return _static_cudaGraphKernelNodeGetAttribute(hNode, attr, value_out) 

1719  

1720  

1721cdef cudaError_t _cudaGraphKernelNodeSetAttribute(cudaGraphNode_t hNode, cudaKernelNodeAttrID attr, const cudaKernelNodeAttrValue* value) except ?cudaErrorCallRequiresNewerDriver nogil: 

1722 return _static_cudaGraphKernelNodeSetAttribute(hNode, attr, value) 

1723  

1724  

1725cdef cudaError_t _cudaGraphAddMemcpyNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaMemcpy3DParms* pCopyParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1726 return _static_cudaGraphAddMemcpyNode(pGraphNode, graph, pDependencies, numDependencies, pCopyParams) 

1727  

1728  

1729cdef cudaError_t _cudaGraphAddMemcpyNode1D(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, void* dst, const void* src, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1730 return _static_cudaGraphAddMemcpyNode1D(pGraphNode, graph, pDependencies, numDependencies, dst, src, count, kind) 

1731  

1732  

1733cdef cudaError_t _cudaGraphMemcpyNodeGetParams(cudaGraphNode_t node, cudaMemcpy3DParms* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1734 return _static_cudaGraphMemcpyNodeGetParams(node, pNodeParams) 

1735  

1736  

1737cdef cudaError_t _cudaGraphMemcpyNodeSetParams(cudaGraphNode_t node, const cudaMemcpy3DParms* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1738 return _static_cudaGraphMemcpyNodeSetParams(node, pNodeParams) 

1739  

1740  

1741cdef cudaError_t _cudaGraphMemcpyNodeSetParams1D(cudaGraphNode_t node, void* dst, const void* src, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1742 return _static_cudaGraphMemcpyNodeSetParams1D(node, dst, src, count, kind) 

1743  

1744  

1745cdef cudaError_t _cudaGraphAddMemsetNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaMemsetParams* pMemsetParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1746 return _static_cudaGraphAddMemsetNode(pGraphNode, graph, pDependencies, numDependencies, pMemsetParams) 

1747  

1748  

1749cdef cudaError_t _cudaGraphMemsetNodeGetParams(cudaGraphNode_t node, cudaMemsetParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1750 return _static_cudaGraphMemsetNodeGetParams(node, pNodeParams) 

1751  

1752  

1753cdef cudaError_t _cudaGraphMemsetNodeSetParams(cudaGraphNode_t node, const cudaMemsetParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1754 return _static_cudaGraphMemsetNodeSetParams(node, pNodeParams) 

1755  

1756  

1757cdef cudaError_t _cudaGraphAddHostNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaHostNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1758 return _static_cudaGraphAddHostNode(pGraphNode, graph, pDependencies, numDependencies, pNodeParams) 

1759  

1760  

1761cdef cudaError_t _cudaGraphHostNodeGetParams(cudaGraphNode_t node, cudaHostNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1762 return _static_cudaGraphHostNodeGetParams(node, pNodeParams) 

1763  

1764  

1765cdef cudaError_t _cudaGraphHostNodeSetParams(cudaGraphNode_t node, const cudaHostNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1766 return _static_cudaGraphHostNodeSetParams(node, pNodeParams) 

1767  

1768  

1769cdef cudaError_t _cudaGraphAddChildGraphNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaGraph_t childGraph) except ?cudaErrorCallRequiresNewerDriver nogil: 

1770 return _static_cudaGraphAddChildGraphNode(pGraphNode, graph, pDependencies, numDependencies, childGraph) 

1771  

1772  

1773cdef cudaError_t _cudaGraphChildGraphNodeGetGraph(cudaGraphNode_t node, cudaGraph_t* pGraph) except ?cudaErrorCallRequiresNewerDriver nogil: 

1774 return _static_cudaGraphChildGraphNodeGetGraph(node, pGraph) 

1775  

1776  

1777cdef cudaError_t _cudaGraphAddEmptyNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies) except ?cudaErrorCallRequiresNewerDriver nogil: 

1778 return _static_cudaGraphAddEmptyNode(pGraphNode, graph, pDependencies, numDependencies) 

1779  

1780  

1781cdef cudaError_t _cudaGraphAddEventRecordNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1782 return _static_cudaGraphAddEventRecordNode(pGraphNode, graph, pDependencies, numDependencies, event) 

1783  

1784  

1785cdef cudaError_t _cudaGraphEventRecordNodeGetEvent(cudaGraphNode_t node, cudaEvent_t* event_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

1786 return _static_cudaGraphEventRecordNodeGetEvent(node, event_out) 

1787  

1788  

1789cdef cudaError_t _cudaGraphEventRecordNodeSetEvent(cudaGraphNode_t node, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1790 return _static_cudaGraphEventRecordNodeSetEvent(node, event) 

1791  

1792  

1793cdef cudaError_t _cudaGraphAddEventWaitNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1794 return _static_cudaGraphAddEventWaitNode(pGraphNode, graph, pDependencies, numDependencies, event) 

1795  

1796  

1797cdef cudaError_t _cudaGraphEventWaitNodeGetEvent(cudaGraphNode_t node, cudaEvent_t* event_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

1798 return _static_cudaGraphEventWaitNodeGetEvent(node, event_out) 

1799  

1800  

1801cdef cudaError_t _cudaGraphEventWaitNodeSetEvent(cudaGraphNode_t node, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1802 return _static_cudaGraphEventWaitNodeSetEvent(node, event) 

1803  

1804  

1805cdef cudaError_t _cudaGraphAddExternalSemaphoresSignalNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaExternalSemaphoreSignalNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1806 return _static_cudaGraphAddExternalSemaphoresSignalNode(pGraphNode, graph, pDependencies, numDependencies, nodeParams) 

1807  

1808  

1809cdef cudaError_t _cudaGraphExternalSemaphoresSignalNodeGetParams(cudaGraphNode_t hNode, cudaExternalSemaphoreSignalNodeParams* params_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

1810 return _static_cudaGraphExternalSemaphoresSignalNodeGetParams(hNode, params_out) 

1811  

1812  

1813cdef cudaError_t _cudaGraphExternalSemaphoresSignalNodeSetParams(cudaGraphNode_t hNode, const cudaExternalSemaphoreSignalNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1814 return _static_cudaGraphExternalSemaphoresSignalNodeSetParams(hNode, nodeParams) 

1815  

1816  

1817cdef cudaError_t _cudaGraphAddExternalSemaphoresWaitNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaExternalSemaphoreWaitNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1818 return _static_cudaGraphAddExternalSemaphoresWaitNode(pGraphNode, graph, pDependencies, numDependencies, nodeParams) 

1819  

1820  

1821cdef cudaError_t _cudaGraphExternalSemaphoresWaitNodeGetParams(cudaGraphNode_t hNode, cudaExternalSemaphoreWaitNodeParams* params_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

1822 return _static_cudaGraphExternalSemaphoresWaitNodeGetParams(hNode, params_out) 

1823  

1824  

1825cdef cudaError_t _cudaGraphExternalSemaphoresWaitNodeSetParams(cudaGraphNode_t hNode, const cudaExternalSemaphoreWaitNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1826 return _static_cudaGraphExternalSemaphoresWaitNodeSetParams(hNode, nodeParams) 

1827  

1828  

1829cdef cudaError_t _cudaGraphAddMemAllocNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaMemAllocNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1830 return _static_cudaGraphAddMemAllocNode(pGraphNode, graph, pDependencies, numDependencies, nodeParams) 

1831  

1832  

1833cdef cudaError_t _cudaGraphMemAllocNodeGetParams(cudaGraphNode_t node, cudaMemAllocNodeParams* params_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

1834 return _static_cudaGraphMemAllocNodeGetParams(node, params_out) 

1835  

1836  

1837cdef cudaError_t _cudaGraphAddMemFreeNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, void* dptr) except ?cudaErrorCallRequiresNewerDriver nogil: 

1838 return _static_cudaGraphAddMemFreeNode(pGraphNode, graph, pDependencies, numDependencies, dptr) 

1839  

1840  

1841cdef cudaError_t _cudaGraphMemFreeNodeGetParams(cudaGraphNode_t node, void* dptr_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

1842 return _static_cudaGraphMemFreeNodeGetParams(node, dptr_out) 

1843  

1844  

1845cdef cudaError_t _cudaDeviceGraphMemTrim(int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

1846 return _static_cudaDeviceGraphMemTrim(device) 

1847  

1848  

1849cdef cudaError_t _cudaDeviceGetGraphMemAttribute(int device, cudaGraphMemAttributeType attr, void* value) except ?cudaErrorCallRequiresNewerDriver nogil: 

1850 return _static_cudaDeviceGetGraphMemAttribute(device, attr, value) 

1851  

1852  

1853cdef cudaError_t _cudaDeviceSetGraphMemAttribute(int device, cudaGraphMemAttributeType attr, void* value) except ?cudaErrorCallRequiresNewerDriver nogil: 

1854 return _static_cudaDeviceSetGraphMemAttribute(device, attr, value) 

1855  

1856  

1857cdef cudaError_t _cudaGraphClone(cudaGraph_t* pGraphClone, cudaGraph_t originalGraph) except ?cudaErrorCallRequiresNewerDriver nogil: 

1858 return _static_cudaGraphClone(pGraphClone, originalGraph) 

1859  

1860  

1861cdef cudaError_t _cudaGraphNodeFindInClone(cudaGraphNode_t* pNode, cudaGraphNode_t originalNode, cudaGraph_t clonedGraph) except ?cudaErrorCallRequiresNewerDriver nogil: 

1862 return _static_cudaGraphNodeFindInClone(pNode, originalNode, clonedGraph) 

1863  

1864  

1865cdef cudaError_t _cudaGraphNodeGetType(cudaGraphNode_t node, cudaGraphNodeType* pType) except ?cudaErrorCallRequiresNewerDriver nogil: 

1866 return _static_cudaGraphNodeGetType(node, pType) 

1867  

1868  

1869cdef cudaError_t _cudaGraphGetNodes(cudaGraph_t graph, cudaGraphNode_t* nodes, size_t* numNodes) except ?cudaErrorCallRequiresNewerDriver nogil: 

1870 return _static_cudaGraphGetNodes(graph, nodes, numNodes) 

1871  

1872  

1873cdef cudaError_t _cudaGraphGetRootNodes(cudaGraph_t graph, cudaGraphNode_t* pRootNodes, size_t* pNumRootNodes) except ?cudaErrorCallRequiresNewerDriver nogil: 

1874 return _static_cudaGraphGetRootNodes(graph, pRootNodes, pNumRootNodes) 

1875  

1876  

1877cdef cudaError_t _cudaGraphGetEdges(cudaGraph_t graph, cudaGraphNode_t* from_, cudaGraphNode_t* to, cudaGraphEdgeData* edgeData, size_t* numEdges) except ?cudaErrorCallRequiresNewerDriver nogil: 

1878 return _static_cudaGraphGetEdges(graph, from_, to, edgeData, numEdges) 

1879  

1880  

1881cdef cudaError_t _cudaGraphNodeGetDependencies(cudaGraphNode_t node, cudaGraphNode_t* pDependencies, cudaGraphEdgeData* edgeData, size_t* pNumDependencies) except ?cudaErrorCallRequiresNewerDriver nogil: 

1882 return _static_cudaGraphNodeGetDependencies(node, pDependencies, edgeData, pNumDependencies) 

1883  

1884  

1885cdef cudaError_t _cudaGraphNodeGetDependentNodes(cudaGraphNode_t node, cudaGraphNode_t* pDependentNodes, cudaGraphEdgeData* edgeData, size_t* pNumDependentNodes) except ?cudaErrorCallRequiresNewerDriver nogil: 

1886 return _static_cudaGraphNodeGetDependentNodes(node, pDependentNodes, edgeData, pNumDependentNodes) 

1887  

1888  

1889cdef cudaError_t _cudaGraphAddDependencies(cudaGraph_t graph, const cudaGraphNode_t* from_, const cudaGraphNode_t* to, const cudaGraphEdgeData* edgeData, size_t numDependencies) except ?cudaErrorCallRequiresNewerDriver nogil: 

1890 return _static_cudaGraphAddDependencies(graph, from_, to, edgeData, numDependencies) 

1891  

1892  

1893cdef cudaError_t _cudaGraphRemoveDependencies(cudaGraph_t graph, const cudaGraphNode_t* from_, const cudaGraphNode_t* to, const cudaGraphEdgeData* edgeData, size_t numDependencies) except ?cudaErrorCallRequiresNewerDriver nogil: 

1894 return _static_cudaGraphRemoveDependencies(graph, from_, to, edgeData, numDependencies) 

1895  

1896  

1897cdef cudaError_t _cudaGraphDestroyNode(cudaGraphNode_t node) except ?cudaErrorCallRequiresNewerDriver nogil: 

1898 return _static_cudaGraphDestroyNode(node) 

1899  

1900  

1901cdef cudaError_t _cudaGraphInstantiate(cudaGraphExec_t* pGraphExec, cudaGraph_t graph, unsigned long long flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1902 return _static_cudaGraphInstantiate(pGraphExec, graph, flags) 

1903  

1904  

1905cdef cudaError_t _cudaGraphInstantiateWithFlags(cudaGraphExec_t* pGraphExec, cudaGraph_t graph, unsigned long long flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1906 return _static_cudaGraphInstantiateWithFlags(pGraphExec, graph, flags) 

1907  

1908  

1909cdef cudaError_t _cudaGraphInstantiateWithParams(cudaGraphExec_t* pGraphExec, cudaGraph_t graph, cudaGraphInstantiateParams* instantiateParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1910 return _static_cudaGraphInstantiateWithParams(pGraphExec, graph, instantiateParams) 

1911  

1912  

1913cdef cudaError_t _cudaGraphExecGetFlags(cudaGraphExec_t graphExec, unsigned long long* flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1914 return _static_cudaGraphExecGetFlags(graphExec, flags) 

1915  

1916  

1917cdef cudaError_t _cudaGraphExecKernelNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaKernelNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1918 return _static_cudaGraphExecKernelNodeSetParams(hGraphExec, node, pNodeParams) 

1919  

1920  

1921cdef cudaError_t _cudaGraphExecMemcpyNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaMemcpy3DParms* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1922 return _static_cudaGraphExecMemcpyNodeSetParams(hGraphExec, node, pNodeParams) 

1923  

1924  

1925cdef cudaError_t _cudaGraphExecMemcpyNodeSetParams1D(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, void* dst, const void* src, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil: 

1926 return _static_cudaGraphExecMemcpyNodeSetParams1D(hGraphExec, node, dst, src, count, kind) 

1927  

1928  

1929cdef cudaError_t _cudaGraphExecMemsetNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaMemsetParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1930 return _static_cudaGraphExecMemsetNodeSetParams(hGraphExec, node, pNodeParams) 

1931  

1932  

1933cdef cudaError_t _cudaGraphExecHostNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaHostNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1934 return _static_cudaGraphExecHostNodeSetParams(hGraphExec, node, pNodeParams) 

1935  

1936  

1937cdef cudaError_t _cudaGraphExecChildGraphNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, cudaGraph_t childGraph) except ?cudaErrorCallRequiresNewerDriver nogil: 

1938 return _static_cudaGraphExecChildGraphNodeSetParams(hGraphExec, node, childGraph) 

1939  

1940  

1941cdef cudaError_t _cudaGraphExecEventRecordNodeSetEvent(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1942 return _static_cudaGraphExecEventRecordNodeSetEvent(hGraphExec, hNode, event) 

1943  

1944  

1945cdef cudaError_t _cudaGraphExecEventWaitNodeSetEvent(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

1946 return _static_cudaGraphExecEventWaitNodeSetEvent(hGraphExec, hNode, event) 

1947  

1948  

1949cdef cudaError_t _cudaGraphExecExternalSemaphoresSignalNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, const cudaExternalSemaphoreSignalNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1950 return _static_cudaGraphExecExternalSemaphoresSignalNodeSetParams(hGraphExec, hNode, nodeParams) 

1951  

1952  

1953cdef cudaError_t _cudaGraphExecExternalSemaphoresWaitNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, const cudaExternalSemaphoreWaitNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

1954 return _static_cudaGraphExecExternalSemaphoresWaitNodeSetParams(hGraphExec, hNode, nodeParams) 

1955  

1956  

1957cdef cudaError_t _cudaGraphNodeSetEnabled(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, unsigned int isEnabled) except ?cudaErrorCallRequiresNewerDriver nogil: 

1958 return _static_cudaGraphNodeSetEnabled(hGraphExec, hNode, isEnabled) 

1959  

1960  

1961cdef cudaError_t _cudaGraphNodeGetEnabled(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, unsigned int* isEnabled) except ?cudaErrorCallRequiresNewerDriver nogil: 

1962 return _static_cudaGraphNodeGetEnabled(hGraphExec, hNode, isEnabled) 

1963  

1964  

1965cdef cudaError_t _cudaGraphExecUpdate(cudaGraphExec_t hGraphExec, cudaGraph_t hGraph, cudaGraphExecUpdateResultInfo* resultInfo) except ?cudaErrorCallRequiresNewerDriver nogil: 

1966 return _static_cudaGraphExecUpdate(hGraphExec, hGraph, resultInfo) 

1967  

1968  

1969cdef cudaError_t _cudaGraphUpload(cudaGraphExec_t graphExec, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1970 return _static_cudaGraphUpload(graphExec, stream) 

1971  

1972  

1973cdef cudaError_t _cudaGraphLaunch(cudaGraphExec_t graphExec, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

1974 return _static_cudaGraphLaunch(graphExec, stream) 

1975  

1976  

1977cdef cudaError_t _cudaGraphExecDestroy(cudaGraphExec_t graphExec) except ?cudaErrorCallRequiresNewerDriver nogil: 

1978 return _static_cudaGraphExecDestroy(graphExec) 

1979  

1980  

1981cdef cudaError_t _cudaGraphDestroy(cudaGraph_t graph) except ?cudaErrorCallRequiresNewerDriver nogil: 

1982 return _static_cudaGraphDestroy(graph) 

1983  

1984  

1985cdef cudaError_t _cudaGraphDebugDotPrint(cudaGraph_t graph, const char* path, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1986 return _static_cudaGraphDebugDotPrint(graph, path, flags) 

1987  

1988  

1989cdef cudaError_t _cudaUserObjectCreate(cudaUserObject_t* object_out, void* ptr, cudaHostFn_t destroy, unsigned int initialRefcount, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

1990 return _static_cudaUserObjectCreate(object_out, ptr, destroy, initialRefcount, flags) 

1991  

1992  

1993cdef cudaError_t _cudaUserObjectRetain(cudaUserObject_t object, unsigned int count) except ?cudaErrorCallRequiresNewerDriver nogil: 

1994 return _static_cudaUserObjectRetain(object, count) 

1995  

1996  

1997cdef cudaError_t _cudaUserObjectRelease(cudaUserObject_t object, unsigned int count) except ?cudaErrorCallRequiresNewerDriver nogil: 

1998 return _static_cudaUserObjectRelease(object, count) 

1999  

2000  

2001cdef cudaError_t _cudaGraphRetainUserObject(cudaGraph_t graph, cudaUserObject_t object, unsigned int count, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

2002 return _static_cudaGraphRetainUserObject(graph, object, count, flags) 

2003  

2004  

2005cdef cudaError_t _cudaGraphReleaseUserObject(cudaGraph_t graph, cudaUserObject_t object, unsigned int count) except ?cudaErrorCallRequiresNewerDriver nogil: 

2006 return _static_cudaGraphReleaseUserObject(graph, object, count) 

2007  

2008  

2009cdef cudaError_t _cudaGraphAddNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, const cudaGraphEdgeData* dependencyData, size_t numDependencies, cudaGraphNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

2010 return _static_cudaGraphAddNode(pGraphNode, graph, pDependencies, dependencyData, numDependencies, nodeParams) 

2011  

2012  

2013cdef cudaError_t _cudaGraphNodeSetParams(cudaGraphNode_t node, cudaGraphNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

2014 return _static_cudaGraphNodeSetParams(node, nodeParams) 

2015  

2016  

2017cdef cudaError_t _cudaGraphExecNodeSetParams(cudaGraphExec_t graphExec, cudaGraphNode_t node, cudaGraphNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

2018 return _static_cudaGraphExecNodeSetParams(graphExec, node, nodeParams) 

2019  

2020  

2021cdef cudaError_t _cudaGraphConditionalHandleCreate(cudaGraphConditionalHandle* pHandle_out, cudaGraph_t graph, unsigned int defaultLaunchValue, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

2022 return _static_cudaGraphConditionalHandleCreate(pHandle_out, graph, defaultLaunchValue, flags) 

2023  

2024  

2025cdef cudaError_t _cudaGetDriverEntryPoint(const char* symbol, void** funcPtr, unsigned long long flags, cudaDriverEntryPointQueryResult* driverStatus) except ?cudaErrorCallRequiresNewerDriver nogil: 

2026 return _static_cudaGetDriverEntryPoint(symbol, funcPtr, flags, driverStatus) 

2027  

2028  

2029cdef cudaError_t _cudaGetDriverEntryPointByVersion(const char* symbol, void** funcPtr, unsigned int cudaVersion, unsigned long long flags, cudaDriverEntryPointQueryResult* driverStatus) except ?cudaErrorCallRequiresNewerDriver nogil: 

2030 return _static_cudaGetDriverEntryPointByVersion(symbol, funcPtr, cudaVersion, flags, driverStatus) 

2031  

2032  

2033cdef cudaError_t _cudaLibraryLoadData(cudaLibrary_t* library, const void* code, cudaJitOption* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, cudaLibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?cudaErrorCallRequiresNewerDriver nogil: 

2034 return _static_cudaLibraryLoadData(library, code, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 

2035  

2036  

2037cdef cudaError_t _cudaLibraryLoadFromFile(cudaLibrary_t* library, const char* fileName, cudaJitOption* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, cudaLibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?cudaErrorCallRequiresNewerDriver nogil: 

2038 return _static_cudaLibraryLoadFromFile(library, fileName, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 

2039  

2040  

2041cdef cudaError_t _cudaLibraryUnload(cudaLibrary_t library) except ?cudaErrorCallRequiresNewerDriver nogil: 

2042 return _static_cudaLibraryUnload(library) 

2043  

2044  

2045cdef cudaError_t _cudaLibraryGetKernel(cudaKernel_t* pKernel, cudaLibrary_t library, const char* name) except ?cudaErrorCallRequiresNewerDriver nogil: 

2046 return _static_cudaLibraryGetKernel(pKernel, library, name) 

2047  

2048  

2049cdef cudaError_t _cudaLibraryGetGlobal(void** dptr, size_t* bytes, cudaLibrary_t library, const char* name) except ?cudaErrorCallRequiresNewerDriver nogil: 

2050 return _static_cudaLibraryGetGlobal(dptr, bytes, library, name) 

2051  

2052  

2053cdef cudaError_t _cudaLibraryGetManaged(void** dptr, size_t* bytes, cudaLibrary_t library, const char* name) except ?cudaErrorCallRequiresNewerDriver nogil: 

2054 return _static_cudaLibraryGetManaged(dptr, bytes, library, name) 

2055  

2056  

2057cdef cudaError_t _cudaLibraryGetUnifiedFunction(void** fptr, cudaLibrary_t library, const char* symbol) except ?cudaErrorCallRequiresNewerDriver nogil: 

2058 return _static_cudaLibraryGetUnifiedFunction(fptr, library, symbol) 

2059  

2060  

2061cdef cudaError_t _cudaLibraryGetKernelCount(unsigned int* count, cudaLibrary_t lib) except ?cudaErrorCallRequiresNewerDriver nogil: 

2062 return _static_cudaLibraryGetKernelCount(count, lib) 

2063  

2064  

2065cdef cudaError_t _cudaLibraryEnumerateKernels(cudaKernel_t* kernels, unsigned int numKernels, cudaLibrary_t lib) except ?cudaErrorCallRequiresNewerDriver nogil: 

2066 return _static_cudaLibraryEnumerateKernels(kernels, numKernels, lib) 

2067  

2068  

2069cdef cudaError_t _cudaKernelSetAttributeForDevice(cudaKernel_t kernel, cudaFuncAttribute attr, int value, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

2070 return _static_cudaKernelSetAttributeForDevice(kernel, attr, value, device) 

2071  

2072  

2073cdef cudaError_t _cudaGetExportTable(const void** ppExportTable, const cudaUUID_t* pExportTableId) except ?cudaErrorCallRequiresNewerDriver nogil: 

2074 return _static_cudaGetExportTable(ppExportTable, pExportTableId) 

2075  

2076  

2077cdef cudaError_t _cudaGetKernel(cudaKernel_t* kernelPtr, const void* entryFuncAddr) except ?cudaErrorCallRequiresNewerDriver nogil: 

2078 return _static_cudaGetKernel(kernelPtr, entryFuncAddr) 

2079  

2080  

2081cdef cudaError_t _cudaProfilerStart() except ?cudaErrorCallRequiresNewerDriver nogil: 

2082 return _static_cudaProfilerStart() 

2083  

2084  

2085cdef cudaError_t _cudaProfilerStop() except ?cudaErrorCallRequiresNewerDriver nogil: 

2086 return _static_cudaProfilerStop() 

2087  

2088  

2089cdef cudaError_t _cudaGetDeviceProperties(cudaDeviceProp* prop, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

2090 return _static_cudaGetDeviceProperties(prop, device) 

2091  

2092  

2093cdef cudaError_t _cudaDeviceGetHostAtomicCapabilities(unsigned int* capabilities, const cudaAtomicOperation* operations, unsigned int count, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

2094 return _static_cudaDeviceGetHostAtomicCapabilities(capabilities, operations, count, device) 

2095  

2096  

2097cdef cudaError_t _cudaDeviceGetP2PAtomicCapabilities(unsigned int* capabilities, const cudaAtomicOperation* operations, unsigned int count, int srcDevice, int dstDevice) except ?cudaErrorCallRequiresNewerDriver nogil: 

2098 return _static_cudaDeviceGetP2PAtomicCapabilities(capabilities, operations, count, srcDevice, dstDevice) 

2099  

2100  

2101cdef cudaError_t _cudaStreamGetCaptureInfo(cudaStream_t stream, cudaStreamCaptureStatus* captureStatus_out, unsigned long long* id_out, cudaGraph_t* graph_out, const cudaGraphNode_t** dependencies_out, const cudaGraphEdgeData** edgeData_out, size_t* numDependencies_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

2102 return _static_cudaStreamGetCaptureInfo(stream, captureStatus_out, id_out, graph_out, dependencies_out, edgeData_out, numDependencies_out) 

2103  

2104  

2105cdef cudaError_t _cudaSignalExternalSemaphoresAsync(const cudaExternalSemaphore_t* extSemArray, const cudaExternalSemaphoreSignalParams* paramsArray, unsigned int numExtSems, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

2106 return _static_cudaSignalExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream) 

2107  

2108  

2109cdef cudaError_t _cudaWaitExternalSemaphoresAsync(const cudaExternalSemaphore_t* extSemArray, const cudaExternalSemaphoreWaitParams* paramsArray, unsigned int numExtSems, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

2110 return _static_cudaWaitExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream) 

2111  

2112  

2113cdef cudaError_t _cudaMemPrefetchBatchAsync(void** dptrs, size_t* sizes, size_t count, cudaMemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

2114 return _static_cudaMemPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, stream) 

2115  

2116  

2117cdef cudaError_t _cudaMemDiscardBatchAsync(void** dptrs, size_t* sizes, size_t count, unsigned long long flags, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

2118 return _static_cudaMemDiscardBatchAsync(dptrs, sizes, count, flags, stream) 

2119  

2120  

2121cdef cudaError_t _cudaMemDiscardAndPrefetchBatchAsync(void** dptrs, size_t* sizes, size_t count, cudaMemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

2122 return _static_cudaMemDiscardAndPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, stream) 

2123  

2124  

2125cdef cudaError_t _cudaMemGetDefaultMemPool(cudaMemPool_t* memPool, cudaMemLocation* location, cudaMemAllocationType type) except ?cudaErrorCallRequiresNewerDriver nogil: 

2126 return _static_cudaMemGetDefaultMemPool(memPool, location, type) 

2127  

2128  

2129cdef cudaError_t _cudaMemGetMemPool(cudaMemPool_t* memPool, cudaMemLocation* location, cudaMemAllocationType type) except ?cudaErrorCallRequiresNewerDriver nogil: 

2130 return _static_cudaMemGetMemPool(memPool, location, type) 

2131  

2132  

2133cdef cudaError_t _cudaMemSetMemPool(cudaMemLocation* location, cudaMemAllocationType type, cudaMemPool_t memPool) except ?cudaErrorCallRequiresNewerDriver nogil: 

2134 return _static_cudaMemSetMemPool(location, type, memPool) 

2135  

2136  

2137cdef cudaError_t _cudaLogsRegisterCallback(cudaLogsCallback_t callbackFunc, void* userData, cudaLogsCallbackHandle* callback_out) except ?cudaErrorCallRequiresNewerDriver nogil: 

2138 return _static_cudaLogsRegisterCallback(callbackFunc, userData, callback_out) 

2139  

2140  

2141cdef cudaError_t _cudaLogsUnregisterCallback(cudaLogsCallbackHandle callback) except ?cudaErrorCallRequiresNewerDriver nogil: 

2142 return _static_cudaLogsUnregisterCallback(callback) 

2143  

2144  

2145cdef cudaError_t _cudaLogsCurrent(cudaLogIterator* iterator_out, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

2146 return _static_cudaLogsCurrent(iterator_out, flags) 

2147  

2148  

2149cdef cudaError_t _cudaLogsDumpToFile(cudaLogIterator* iterator, const char* pathToFile, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

2150 return _static_cudaLogsDumpToFile(iterator, pathToFile, flags) 

2151  

2152  

2153cdef cudaError_t _cudaLogsDumpToMemory(cudaLogIterator* iterator, char* buffer, size_t* size, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

2154 return _static_cudaLogsDumpToMemory(iterator, buffer, size, flags) 

2155  

2156  

2157cdef cudaError_t _cudaGraphNodeGetContainingGraph(cudaGraphNode_t hNode, cudaGraph_t* phGraph) except ?cudaErrorCallRequiresNewerDriver nogil: 

2158 return _static_cudaGraphNodeGetContainingGraph(hNode, phGraph) 

2159  

2160  

2161cdef cudaError_t _cudaGraphNodeGetLocalId(cudaGraphNode_t hNode, unsigned int* nodeId) except ?cudaErrorCallRequiresNewerDriver nogil: 

2162 return _static_cudaGraphNodeGetLocalId(hNode, nodeId) 

2163  

2164  

2165cdef cudaError_t _cudaGraphNodeGetToolsId(cudaGraphNode_t hNode, unsigned long long* toolsNodeId) except ?cudaErrorCallRequiresNewerDriver nogil: 

2166 return _static_cudaGraphNodeGetToolsId(hNode, toolsNodeId) 

2167  

2168  

2169cdef cudaError_t _cudaGraphGetId(cudaGraph_t hGraph, unsigned int* graphID) except ?cudaErrorCallRequiresNewerDriver nogil: 

2170 return _static_cudaGraphGetId(hGraph, graphID) 

2171  

2172  

2173cdef cudaError_t _cudaGraphExecGetId(cudaGraphExec_t hGraphExec, unsigned int* graphID) except ?cudaErrorCallRequiresNewerDriver nogil: 

2174 return _static_cudaGraphExecGetId(hGraphExec, graphID) 

2175  

2176  

2177cdef cudaError_t _cudaGraphConditionalHandleCreate_v2(cudaGraphConditionalHandle* pHandle_out, cudaGraph_t graph, cudaExecutionContext_t ctx, unsigned int defaultLaunchValue, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

2178 return _static_cudaGraphConditionalHandleCreate_v2(pHandle_out, graph, ctx, defaultLaunchValue, flags) 

2179  

2180  

2181cdef cudaError_t _cudaDeviceGetDevResource(int device, cudaDevResource* resource, cudaDevResourceType type) except ?cudaErrorCallRequiresNewerDriver nogil: 

2182 return _static_cudaDeviceGetDevResource(device, resource, type) 

2183  

2184  

2185cdef cudaError_t _cudaDevSmResourceSplitByCount(cudaDevResource* result, unsigned int* nbGroups, const cudaDevResource* input, cudaDevResource* remaining, unsigned int flags, unsigned int minCount) except ?cudaErrorCallRequiresNewerDriver nogil: 

2186 return _static_cudaDevSmResourceSplitByCount(result, nbGroups, input, remaining, flags, minCount) 

2187  

2188  

2189cdef cudaError_t _cudaDevSmResourceSplit(cudaDevResource* result, unsigned int nbGroups, const cudaDevResource* input, cudaDevResource* remainder, unsigned int flags, cudaDevSmResourceGroupParams* groupParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

2190 return _static_cudaDevSmResourceSplit(result, nbGroups, input, remainder, flags, groupParams) 

2191  

2192  

2193cdef cudaError_t _cudaDevResourceGenerateDesc(cudaDevResourceDesc_t* phDesc, cudaDevResource* resources, unsigned int nbResources) except ?cudaErrorCallRequiresNewerDriver nogil: 

2194 return _static_cudaDevResourceGenerateDesc(phDesc, resources, nbResources) 

2195  

2196  

2197cdef cudaError_t _cudaGreenCtxCreate(cudaExecutionContext_t* phCtx, cudaDevResourceDesc_t desc, int device, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil: 

2198 return _static_cudaGreenCtxCreate(phCtx, desc, device, flags) 

2199  

2200  

2201cdef cudaError_t _cudaExecutionCtxDestroy(cudaExecutionContext_t ctx) except ?cudaErrorCallRequiresNewerDriver nogil: 

2202 return _static_cudaExecutionCtxDestroy(ctx) 

2203  

2204  

2205cdef cudaError_t _cudaExecutionCtxGetDevResource(cudaExecutionContext_t ctx, cudaDevResource* resource, cudaDevResourceType type) except ?cudaErrorCallRequiresNewerDriver nogil: 

2206 return _static_cudaExecutionCtxGetDevResource(ctx, resource, type) 

2207  

2208  

2209cdef cudaError_t _cudaExecutionCtxGetDevice(int* device, cudaExecutionContext_t ctx) except ?cudaErrorCallRequiresNewerDriver nogil: 

2210 return _static_cudaExecutionCtxGetDevice(device, ctx) 

2211  

2212  

2213cdef cudaError_t _cudaExecutionCtxGetId(cudaExecutionContext_t ctx, unsigned long long* ctxId) except ?cudaErrorCallRequiresNewerDriver nogil: 

2214 return _static_cudaExecutionCtxGetId(ctx, ctxId) 

2215  

2216  

2217cdef cudaError_t _cudaExecutionCtxStreamCreate(cudaStream_t* phStream, cudaExecutionContext_t ctx, unsigned int flags, int priority) except ?cudaErrorCallRequiresNewerDriver nogil: 

2218 return _static_cudaExecutionCtxStreamCreate(phStream, ctx, flags, priority) 

2219  

2220  

2221cdef cudaError_t _cudaExecutionCtxSynchronize(cudaExecutionContext_t ctx) except ?cudaErrorCallRequiresNewerDriver nogil: 

2222 return _static_cudaExecutionCtxSynchronize(ctx) 

2223  

2224  

2225cdef cudaError_t _cudaStreamGetDevResource(cudaStream_t hStream, cudaDevResource* resource, cudaDevResourceType type) except ?cudaErrorCallRequiresNewerDriver nogil: 

2226 return _static_cudaStreamGetDevResource(hStream, resource, type) 

2227  

2228  

2229cdef cudaError_t _cudaExecutionCtxRecordEvent(cudaExecutionContext_t ctx, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

2230 return _static_cudaExecutionCtxRecordEvent(ctx, event) 

2231  

2232  

2233cdef cudaError_t _cudaExecutionCtxWaitEvent(cudaExecutionContext_t ctx, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil: 

2234 return _static_cudaExecutionCtxWaitEvent(ctx, event) 

2235  

2236  

2237cdef cudaError_t _cudaDeviceGetExecutionCtx(cudaExecutionContext_t* ctx, int device) except ?cudaErrorCallRequiresNewerDriver nogil: 

2238 return _static_cudaDeviceGetExecutionCtx(ctx, device) 

2239  

2240  

2241cdef cudaError_t _cudaFuncGetParamCount(const void* func, size_t* paramCount) except ?cudaErrorCallRequiresNewerDriver nogil: 

2242 return _static_cudaFuncGetParamCount(func, paramCount) 

2243  

2244  

2245cdef cudaError_t _cudaLaunchHostFunc_v2(cudaStream_t stream, cudaHostFn_t fn, void* userData, unsigned int syncMode) except ?cudaErrorCallRequiresNewerDriver nogil: 

2246 return _static_cudaLaunchHostFunc_v2(stream, fn, userData, syncMode) 

2247  

2248  

2249cdef cudaError_t _cudaMemcpyWithAttributesAsync(void* dst, const void* src, size_t size, cudaMemcpyAttributes* attr, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

2250 return _static_cudaMemcpyWithAttributesAsync(dst, src, size, attr, stream) 

2251  

2252  

2253cdef cudaError_t _cudaMemcpy3DWithAttributesAsync(cudaMemcpy3DBatchOp* op, unsigned long long flags, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil: 

2254 return _static_cudaMemcpy3DWithAttributesAsync(op, flags, stream) 

2255  

2256  

2257cdef cudaError_t _cudaGraphNodeGetParams(cudaGraphNode_t node, cudaGraphNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil: 

2258 return _static_cudaGraphNodeGetParams(node, nodeParams) 

2259  

2260  

2261cdef cudaError_t _cudaStreamBeginRecaptureToGraph(cudaStream_t stream, cudaStreamCaptureMode mode, cudaGraph_t graph, cudaGraphRecaptureCallbackData* callbackData) except ?cudaErrorCallRequiresNewerDriver nogil: 

2262 return _static_cudaStreamBeginRecaptureToGraph(stream, mode, graph, callbackData)