# Copyright 2021-2024 NVIDIA Corporation. All rights reserved. # # Please refer to the NVIDIA end user license agreement (EULA) associated # with this source code for terms and conditions that govern your use of # this software. Any use, reproduction, disclosure, or distribution of # this software and related documentation outside the terms of the EULA # is strictly prohibited. from libc.stdint cimport uint32_t, uint64_t cdef extern from "vector_types.h": cdef struct dim3: unsigned int x unsigned int y unsigned int z cdef extern from "driver_types.h": cdef enum cudaError: cudaSuccess = 0 cudaErrorInvalidValue = 1 cudaErrorMemoryAllocation = 2 cudaErrorInitializationError = 3 cudaErrorCudartUnloading = 4 cudaErrorProfilerDisabled = 5 cudaErrorProfilerNotInitialized = 6 cudaErrorProfilerAlreadyStarted = 7 cudaErrorProfilerAlreadyStopped = 8 cudaErrorInvalidConfiguration = 9 cudaErrorInvalidPitchValue = 12 cudaErrorInvalidSymbol = 13 cudaErrorInvalidHostPointer = 16 cudaErrorInvalidDevicePointer = 17 cudaErrorInvalidTexture = 18 cudaErrorInvalidTextureBinding = 19 cudaErrorInvalidChannelDescriptor = 20 cudaErrorInvalidMemcpyDirection = 21 cudaErrorAddressOfConstant = 22 cudaErrorTextureFetchFailed = 23 cudaErrorTextureNotBound = 24 cudaErrorSynchronizationError = 25 cudaErrorInvalidFilterSetting = 26 cudaErrorInvalidNormSetting = 27 cudaErrorMixedDeviceExecution = 28 cudaErrorNotYetImplemented = 31 cudaErrorMemoryValueTooLarge = 32 cudaErrorStubLibrary = 34 cudaErrorInsufficientDriver = 35 cudaErrorCallRequiresNewerDriver = 36 cudaErrorInvalidSurface = 37 cudaErrorDuplicateVariableName = 43 cudaErrorDuplicateTextureName = 44 cudaErrorDuplicateSurfaceName = 45 cudaErrorDevicesUnavailable = 46 cudaErrorIncompatibleDriverContext = 49 cudaErrorMissingConfiguration = 52 cudaErrorPriorLaunchFailure = 53 cudaErrorLaunchMaxDepthExceeded = 65 cudaErrorLaunchFileScopedTex = 66 cudaErrorLaunchFileScopedSurf = 67 cudaErrorSyncDepthExceeded = 68 cudaErrorLaunchPendingCountExceeded = 69 cudaErrorInvalidDeviceFunction = 98 cudaErrorNoDevice = 100 cudaErrorInvalidDevice = 101 cudaErrorDeviceNotLicensed = 102 cudaErrorSoftwareValidityNotEstablished = 103 cudaErrorStartupFailure = 127 cudaErrorInvalidKernelImage = 200 cudaErrorDeviceUninitialized = 201 cudaErrorMapBufferObjectFailed = 205 cudaErrorUnmapBufferObjectFailed = 206 cudaErrorArrayIsMapped = 207 cudaErrorAlreadyMapped = 208 cudaErrorNoKernelImageForDevice = 209 cudaErrorAlreadyAcquired = 210 cudaErrorNotMapped = 211 cudaErrorNotMappedAsArray = 212 cudaErrorNotMappedAsPointer = 213 cudaErrorECCUncorrectable = 214 cudaErrorUnsupportedLimit = 215 cudaErrorDeviceAlreadyInUse = 216 cudaErrorPeerAccessUnsupported = 217 cudaErrorInvalidPtx = 218 cudaErrorInvalidGraphicsContext = 219 cudaErrorNvlinkUncorrectable = 220 cudaErrorJitCompilerNotFound = 221 cudaErrorUnsupportedPtxVersion = 222 cudaErrorJitCompilationDisabled = 223 cudaErrorUnsupportedExecAffinity = 224 cudaErrorUnsupportedDevSideSync = 225 cudaErrorInvalidSource = 300 cudaErrorFileNotFound = 301 cudaErrorSharedObjectSymbolNotFound = 302 cudaErrorSharedObjectInitFailed = 303 cudaErrorOperatingSystem = 304 cudaErrorInvalidResourceHandle = 400 cudaErrorIllegalState = 401 cudaErrorLossyQuery = 402 cudaErrorSymbolNotFound = 500 cudaErrorNotReady = 600 cudaErrorIllegalAddress = 700 cudaErrorLaunchOutOfResources = 701 cudaErrorLaunchTimeout = 702 cudaErrorLaunchIncompatibleTexturing = 703 cudaErrorPeerAccessAlreadyEnabled = 704 cudaErrorPeerAccessNotEnabled = 705 cudaErrorSetOnActiveProcess = 708 cudaErrorContextIsDestroyed = 709 cudaErrorAssert = 710 cudaErrorTooManyPeers = 711 cudaErrorHostMemoryAlreadyRegistered = 712 cudaErrorHostMemoryNotRegistered = 713 cudaErrorHardwareStackError = 714 cudaErrorIllegalInstruction = 715 cudaErrorMisalignedAddress = 716 cudaErrorInvalidAddressSpace = 717 cudaErrorInvalidPc = 718 cudaErrorLaunchFailure = 719 cudaErrorCooperativeLaunchTooLarge = 720 cudaErrorNotPermitted = 800 cudaErrorNotSupported = 801 cudaErrorSystemNotReady = 802 cudaErrorSystemDriverMismatch = 803 cudaErrorCompatNotSupportedOnDevice = 804 cudaErrorMpsConnectionFailed = 805 cudaErrorMpsRpcFailure = 806 cudaErrorMpsServerNotReady = 807 cudaErrorMpsMaxClientsReached = 808 cudaErrorMpsMaxConnectionsReached = 809 cudaErrorMpsClientTerminated = 810 cudaErrorCdpNotSupported = 811 cudaErrorCdpVersionMismatch = 812 cudaErrorStreamCaptureUnsupported = 900 cudaErrorStreamCaptureInvalidated = 901 cudaErrorStreamCaptureMerge = 902 cudaErrorStreamCaptureUnmatched = 903 cudaErrorStreamCaptureUnjoined = 904 cudaErrorStreamCaptureIsolation = 905 cudaErrorStreamCaptureImplicit = 906 cudaErrorCapturedEvent = 907 cudaErrorStreamCaptureWrongThread = 908 cudaErrorTimeout = 909 cudaErrorGraphExecUpdateFailure = 910 cudaErrorExternalDevice = 911 cudaErrorInvalidClusterSize = 912 cudaErrorFunctionNotLoaded = 913 cudaErrorInvalidResourceType = 914 cudaErrorInvalidResourceConfiguration = 915 cudaErrorUnknown = 999 cudaErrorApiFailureBase = 10000 ctypedef cudaError cudaError_t cdef struct cudaChannelFormatDesc: int x int y int z int w cudaChannelFormatKind f cdef struct cudaArray: pass ctypedef cudaArray* cudaArray_t cdef struct cudaArray: pass ctypedef cudaArray* cudaArray_const_t cdef struct cudaMipmappedArray: pass ctypedef cudaMipmappedArray* cudaMipmappedArray_t cdef struct cudaMipmappedArray: pass ctypedef cudaMipmappedArray* cudaMipmappedArray_const_t cdef struct anon_struct0: unsigned int width unsigned int height unsigned int depth cdef struct cudaArraySparseProperties: anon_struct0 tileExtent unsigned int miptailFirstLevel unsigned long long miptailSize unsigned int flags unsigned int reserved[4] cdef struct cudaArrayMemoryRequirements: size_t size size_t alignment unsigned int reserved[4] cdef struct cudaPitchedPtr: void* ptr size_t pitch size_t xsize size_t ysize cdef struct cudaExtent: size_t width size_t height size_t depth cdef struct cudaPos: size_t x size_t y size_t z cdef struct cudaMemcpy3DParms: cudaArray_t srcArray cudaPos srcPos cudaPitchedPtr srcPtr cudaArray_t dstArray cudaPos dstPos cudaPitchedPtr dstPtr cudaExtent extent cudaMemcpyKind kind cdef struct cudaMemcpyNodeParams: int flags int reserved[3] cudaMemcpy3DParms copyParams cdef struct cudaMemcpy3DPeerParms: cudaArray_t srcArray cudaPos srcPos cudaPitchedPtr srcPtr int srcDevice cudaArray_t dstArray cudaPos dstPos cudaPitchedPtr dstPtr int dstDevice cudaExtent extent cdef struct cudaMemsetParams: void* dst size_t pitch unsigned int value unsigned int elementSize size_t width size_t height cdef struct cudaMemsetParamsV2: void* dst size_t pitch unsigned int value unsigned int elementSize size_t width size_t height cdef struct cudaAccessPolicyWindow: void* base_ptr size_t num_bytes float hitRatio cudaAccessProperty hitProp cudaAccessProperty missProp ctypedef void (*cudaHostFn_t)(void* userData) cdef struct cudaHostNodeParams: cudaHostFn_t fn void* userData cdef struct cudaHostNodeParamsV2: cudaHostFn_t fn void* userData cdef struct anon_struct1: cudaArray_t array cdef struct anon_struct2: cudaMipmappedArray_t mipmap cdef struct anon_struct3: void* devPtr cudaChannelFormatDesc desc size_t sizeInBytes cdef struct anon_struct4: void* devPtr cudaChannelFormatDesc desc size_t width size_t height size_t pitchInBytes cdef union anon_union0: anon_struct1 array anon_struct2 mipmap anon_struct3 linear anon_struct4 pitch2D cdef struct cudaResourceDesc: cudaResourceType resType anon_union0 res cdef struct cudaResourceViewDesc: cudaResourceViewFormat format size_t width size_t height size_t depth unsigned int firstMipmapLevel unsigned int lastMipmapLevel unsigned int firstLayer unsigned int lastLayer cdef struct cudaPointerAttributes: cudaMemoryType type int device void* devicePointer void* hostPointer cdef struct cudaFuncAttributes: size_t sharedSizeBytes size_t constSizeBytes size_t localSizeBytes int maxThreadsPerBlock int numRegs int ptxVersion int binaryVersion int cacheModeCA int maxDynamicSharedSizeBytes int preferredShmemCarveout int clusterDimMustBeSet int requiredClusterWidth int requiredClusterHeight int requiredClusterDepth int clusterSchedulingPolicyPreference int nonPortableClusterSizeAllowed int reserved[16] cdef struct cudaMemLocation: cudaMemLocationType type int id cdef struct cudaMemAccessDesc: cudaMemLocation location cudaMemAccessFlags flags cdef struct cudaMemPoolProps: cudaMemAllocationType allocType cudaMemAllocationHandleType handleTypes cudaMemLocation location void* win32SecurityAttributes size_t maxSize unsigned short usage unsigned char reserved[54] cdef struct cudaMemPoolPtrExportData: unsigned char reserved[64] cdef struct cudaMemAllocNodeParams: cudaMemPoolProps poolProps const cudaMemAccessDesc* accessDescs size_t accessDescCount size_t bytesize void* dptr cdef struct cudaMemAllocNodeParamsV2: cudaMemPoolProps poolProps const cudaMemAccessDesc* accessDescs size_t accessDescCount size_t bytesize void* dptr cdef struct cudaMemFreeNodeParams: void* dptr cdef struct CUuuid_st: char bytes[16] ctypedef CUuuid_st CUuuid ctypedef CUuuid_st cudaUUID_t cdef struct cudaDeviceProp: char name[256] cudaUUID_t uuid char luid[8] unsigned int luidDeviceNodeMask size_t totalGlobalMem size_t sharedMemPerBlock int regsPerBlock int warpSize size_t memPitch int maxThreadsPerBlock int maxThreadsDim[3] int maxGridSize[3] int clockRate size_t totalConstMem int major int minor size_t textureAlignment size_t texturePitchAlignment int deviceOverlap int multiProcessorCount int kernelExecTimeoutEnabled int integrated int canMapHostMemory int computeMode int maxTexture1D int maxTexture1DMipmap int maxTexture1DLinear int maxTexture2D[2] int maxTexture2DMipmap[2] int maxTexture2DLinear[3] int maxTexture2DGather[2] int maxTexture3D[3] int maxTexture3DAlt[3] int maxTextureCubemap int maxTexture1DLayered[2] int maxTexture2DLayered[3] int maxTextureCubemapLayered[2] int maxSurface1D int maxSurface2D[2] int maxSurface3D[3] int maxSurface1DLayered[2] int maxSurface2DLayered[3] int maxSurfaceCubemap int maxSurfaceCubemapLayered[2] size_t surfaceAlignment int concurrentKernels int ECCEnabled int pciBusID int pciDeviceID int pciDomainID int tccDriver int asyncEngineCount int unifiedAddressing int memoryClockRate int memoryBusWidth int l2CacheSize int persistingL2CacheMaxSize int maxThreadsPerMultiProcessor int streamPrioritiesSupported int globalL1CacheSupported int localL1CacheSupported size_t sharedMemPerMultiprocessor int regsPerMultiprocessor int managedMemory int isMultiGpuBoard int multiGpuBoardGroupID int hostNativeAtomicSupported int singleToDoublePrecisionPerfRatio int pageableMemoryAccess int concurrentManagedAccess int computePreemptionSupported int canUseHostPointerForRegisteredMem int cooperativeLaunch int cooperativeMultiDeviceLaunch size_t sharedMemPerBlockOptin int pageableMemoryAccessUsesHostPageTables int directManagedMemAccessFromHost int maxBlocksPerMultiProcessor int accessPolicyMaxWindowSize size_t reservedSharedMemPerBlock int hostRegisterSupported int sparseCudaArraySupported int hostRegisterReadOnlySupported int timelineSemaphoreInteropSupported int memoryPoolsSupported int gpuDirectRDMASupported unsigned int gpuDirectRDMAFlushWritesOptions int gpuDirectRDMAWritesOrdering unsigned int memoryPoolSupportedHandleTypes int deferredMappingCudaArraySupported int ipcEventSupported int clusterLaunch int unifiedFunctionPointers int reserved2[2] int reserved1[1] int reserved[60] cdef struct cudaIpcEventHandle_st: char reserved[64] ctypedef cudaIpcEventHandle_st cudaIpcEventHandle_t cdef struct cudaIpcMemHandle_st: char reserved[64] ctypedef cudaIpcMemHandle_st cudaIpcMemHandle_t cdef struct cudaMemFabricHandle_st: char reserved[64] ctypedef cudaMemFabricHandle_st cudaMemFabricHandle_t cdef struct anon_struct5: void* handle const void* name cdef union anon_union1: int fd anon_struct5 win32 const void* nvSciBufObject cdef struct cudaExternalMemoryHandleDesc: cudaExternalMemoryHandleType type anon_union1 handle unsigned long long size unsigned int flags cdef struct cudaExternalMemoryBufferDesc: unsigned long long offset unsigned long long size unsigned int flags cdef struct cudaExternalMemoryMipmappedArrayDesc: unsigned long long offset cudaChannelFormatDesc formatDesc cudaExtent extent unsigned int flags unsigned int numLevels cdef struct anon_struct6: void* handle const void* name cdef union anon_union2: int fd anon_struct6 win32 const void* nvSciSyncObj cdef struct cudaExternalSemaphoreHandleDesc: cudaExternalSemaphoreHandleType type anon_union2 handle unsigned int flags cdef struct anon_struct13: unsigned long long value cdef union anon_union5: void* fence unsigned long long reserved cdef struct anon_struct14: unsigned long long key cdef struct anon_struct15: anon_struct13 fence anon_union5 nvSciSync anon_struct14 keyedMutex unsigned int reserved[12] cdef struct cudaExternalSemaphoreSignalParams: anon_struct15 params unsigned int flags unsigned int reserved[16] cdef struct anon_struct16: unsigned long long value cdef union anon_union6: void* fence unsigned long long reserved cdef struct anon_struct17: unsigned long long key unsigned int timeoutMs cdef struct anon_struct18: anon_struct16 fence anon_union6 nvSciSync anon_struct17 keyedMutex unsigned int reserved[10] cdef struct cudaExternalSemaphoreWaitParams: anon_struct18 params unsigned int flags unsigned int reserved[16] cdef struct CUstream_st: pass ctypedef CUstream_st* cudaStream_t cdef struct CUevent_st: pass ctypedef CUevent_st* cudaEvent_t cdef struct cudaGraphicsResource: pass ctypedef cudaGraphicsResource* cudaGraphicsResource_t cdef struct CUexternalMemory_st: pass ctypedef CUexternalMemory_st* cudaExternalMemory_t cdef struct CUexternalSemaphore_st: pass ctypedef CUexternalSemaphore_st* cudaExternalSemaphore_t cdef struct CUgraph_st: pass ctypedef CUgraph_st* cudaGraph_t cdef struct CUgraphNode_st: pass ctypedef CUgraphNode_st* cudaGraphNode_t cdef struct CUuserObject_st: pass ctypedef CUuserObject_st* cudaUserObject_t ctypedef unsigned long long cudaGraphConditionalHandle cdef struct CUfunc_st: pass ctypedef CUfunc_st* cudaFunction_t cdef struct CUkern_st: pass ctypedef CUkern_st* cudaKernel_t cdef struct CUmemPoolHandle_st: pass ctypedef CUmemPoolHandle_st* cudaMemPool_t cdef struct cudaKernelNodeParams: void* func dim3 gridDim dim3 blockDim unsigned int sharedMemBytes void** kernelParams void** extra cdef struct cudaKernelNodeParamsV2: void* func dim3 gridDim dim3 blockDim unsigned int sharedMemBytes void** kernelParams void** extra cdef struct cudaExternalSemaphoreSignalNodeParams: cudaExternalSemaphore_t* extSemArray const cudaExternalSemaphoreSignalParams* paramsArray unsigned int numExtSems cdef struct cudaExternalSemaphoreSignalNodeParamsV2: cudaExternalSemaphore_t* extSemArray const cudaExternalSemaphoreSignalParams* paramsArray unsigned int numExtSems cdef struct cudaExternalSemaphoreWaitNodeParams: cudaExternalSemaphore_t* extSemArray const cudaExternalSemaphoreWaitParams* paramsArray unsigned int numExtSems cdef struct cudaExternalSemaphoreWaitNodeParamsV2: cudaExternalSemaphore_t* extSemArray const cudaExternalSemaphoreWaitParams* paramsArray unsigned int numExtSems cdef struct cudaConditionalNodeParams: cudaGraphConditionalHandle handle cudaGraphConditionalNodeType type unsigned int size cudaGraph_t* phGraph_out cdef struct cudaChildGraphNodeParams: cudaGraph_t graph cdef struct cudaEventRecordNodeParams: cudaEvent_t event cdef struct cudaEventWaitNodeParams: cudaEvent_t event cdef struct cudaGraphNodeParams: cudaGraphNodeType type int reserved0[3] long long reserved1[29] cudaKernelNodeParamsV2 kernel cudaMemcpyNodeParams memcpy cudaMemsetParamsV2 memset cudaHostNodeParamsV2 host cudaChildGraphNodeParams graph cudaEventWaitNodeParams eventWait cudaEventRecordNodeParams eventRecord cudaExternalSemaphoreSignalNodeParamsV2 extSemSignal cudaExternalSemaphoreWaitNodeParamsV2 extSemWait cudaMemAllocNodeParamsV2 alloc cudaMemFreeNodeParams free cudaConditionalNodeParams conditional long long reserved2 cdef enum cudaGraphDependencyType_enum: cudaGraphDependencyTypeDefault = 0 cudaGraphDependencyTypeProgrammatic = 1 ctypedef cudaGraphDependencyType_enum cudaGraphDependencyType cdef struct cudaGraphEdgeData_st: unsigned char from_port unsigned char to_port unsigned char type unsigned char reserved[5] ctypedef cudaGraphEdgeData_st cudaGraphEdgeData cdef struct CUgraphExec_st: pass ctypedef CUgraphExec_st* cudaGraphExec_t cdef enum cudaGraphInstantiateResult: cudaGraphInstantiateSuccess = 0 cudaGraphInstantiateError = 1 cudaGraphInstantiateInvalidStructure = 2 cudaGraphInstantiateNodeOperationNotSupported = 3 cudaGraphInstantiateMultipleDevicesNotSupported = 4 cdef struct cudaGraphInstantiateParams_st: unsigned long long flags cudaStream_t uploadStream cudaGraphNode_t errNode_out cudaGraphInstantiateResult result_out ctypedef cudaGraphInstantiateParams_st cudaGraphInstantiateParams cdef struct cudaGraphExecUpdateResultInfo_st: cudaGraphExecUpdateResult result cudaGraphNode_t errorNode cudaGraphNode_t errorFromNode ctypedef cudaGraphExecUpdateResultInfo_st cudaGraphExecUpdateResultInfo cdef struct CUgraphDeviceUpdatableNode_st: pass ctypedef CUgraphDeviceUpdatableNode_st* cudaGraphDeviceNode_t cdef struct anon_struct19: const void* pValue size_t offset size_t size cdef union anon_union8: dim3 gridDim anon_struct19 param unsigned int isEnabled cdef struct cudaGraphKernelNodeUpdate: cudaGraphDeviceNode_t node cudaGraphKernelNodeField field anon_union8 updateData cdef enum cudaLaunchMemSyncDomain: cudaLaunchMemSyncDomainDefault = 0 cudaLaunchMemSyncDomainRemote = 1 cdef struct cudaLaunchMemSyncDomainMap_st: unsigned char default_ unsigned char remote ctypedef cudaLaunchMemSyncDomainMap_st cudaLaunchMemSyncDomainMap cdef enum cudaLaunchAttributeID: cudaLaunchAttributeIgnore = 0 cudaLaunchAttributeAccessPolicyWindow = 1 cudaLaunchAttributeCooperative = 2 cudaLaunchAttributeSynchronizationPolicy = 3 cudaLaunchAttributeClusterDimension = 4 cudaLaunchAttributeClusterSchedulingPolicyPreference = 5 cudaLaunchAttributeProgrammaticStreamSerialization = 6 cudaLaunchAttributeProgrammaticEvent = 7 cudaLaunchAttributePriority = 8 cudaLaunchAttributeMemSyncDomainMap = 9 cudaLaunchAttributeMemSyncDomain = 10 cudaLaunchAttributeLaunchCompletionEvent = 12 cudaLaunchAttributeDeviceUpdatableKernelNode = 13 cudaLaunchAttributePreferredSharedMemoryCarveout = 14 cdef struct anon_struct20: unsigned int x unsigned int y unsigned int z cdef struct anon_struct21: cudaEvent_t event int flags int triggerAtBlockStart cdef struct anon_struct22: cudaEvent_t event int flags cdef struct anon_struct23: int deviceUpdatable cudaGraphDeviceNode_t devNode cdef union cudaLaunchAttributeValue: char pad[64] cudaAccessPolicyWindow accessPolicyWindow int cooperative cudaSynchronizationPolicy syncPolicy anon_struct20 clusterDim cudaClusterSchedulingPolicy clusterSchedulingPolicyPreference int programmaticStreamSerializationAllowed anon_struct21 programmaticEvent int priority cudaLaunchMemSyncDomainMap memSyncDomainMap cudaLaunchMemSyncDomain memSyncDomain anon_struct22 launchCompletionEvent anon_struct23 deviceUpdatableKernelNode unsigned int sharedMemCarveout cdef struct cudaLaunchAttribute_st: cudaLaunchAttributeID id cudaLaunchAttributeValue val ctypedef cudaLaunchAttribute_st cudaLaunchAttribute cdef struct cudaAsyncCallbackEntry: pass ctypedef cudaAsyncCallbackEntry* cudaAsyncCallbackHandle_t cdef enum cudaAsyncNotificationType_enum: cudaAsyncNotificationTypeOverBudget = 1 ctypedef cudaAsyncNotificationType_enum cudaAsyncNotificationType cdef struct anon_struct24: unsigned long long bytesOverBudget cdef union anon_union9: anon_struct24 overBudget cdef struct cudaAsyncNotificationInfo: cudaAsyncNotificationType type anon_union9 info ctypedef cudaAsyncNotificationInfo cudaAsyncNotificationInfo_t ctypedef void (*cudaAsyncCallback)(cudaAsyncNotificationInfo_t* , void* , cudaAsyncCallbackHandle_t ) cdef enum cudaChannelFormatKind: cudaChannelFormatKindSigned = 0 cudaChannelFormatKindUnsigned = 1 cudaChannelFormatKindFloat = 2 cudaChannelFormatKindNone = 3 cudaChannelFormatKindNV12 = 4 cudaChannelFormatKindUnsignedNormalized8X1 = 5 cudaChannelFormatKindUnsignedNormalized8X2 = 6 cudaChannelFormatKindUnsignedNormalized8X4 = 7 cudaChannelFormatKindUnsignedNormalized16X1 = 8 cudaChannelFormatKindUnsignedNormalized16X2 = 9 cudaChannelFormatKindUnsignedNormalized16X4 = 10 cudaChannelFormatKindSignedNormalized8X1 = 11 cudaChannelFormatKindSignedNormalized8X2 = 12 cudaChannelFormatKindSignedNormalized8X4 = 13 cudaChannelFormatKindSignedNormalized16X1 = 14 cudaChannelFormatKindSignedNormalized16X2 = 15 cudaChannelFormatKindSignedNormalized16X4 = 16 cudaChannelFormatKindUnsignedBlockCompressed1 = 17 cudaChannelFormatKindUnsignedBlockCompressed1SRGB = 18 cudaChannelFormatKindUnsignedBlockCompressed2 = 19 cudaChannelFormatKindUnsignedBlockCompressed2SRGB = 20 cudaChannelFormatKindUnsignedBlockCompressed3 = 21 cudaChannelFormatKindUnsignedBlockCompressed3SRGB = 22 cudaChannelFormatKindUnsignedBlockCompressed4 = 23 cudaChannelFormatKindSignedBlockCompressed4 = 24 cudaChannelFormatKindUnsignedBlockCompressed5 = 25 cudaChannelFormatKindSignedBlockCompressed5 = 26 cudaChannelFormatKindUnsignedBlockCompressed6H = 27 cudaChannelFormatKindSignedBlockCompressed6H = 28 cudaChannelFormatKindUnsignedBlockCompressed7 = 29 cudaChannelFormatKindUnsignedBlockCompressed7SRGB = 30 cdef enum cudaMemoryType: cudaMemoryTypeUnregistered = 0 cudaMemoryTypeHost = 1 cudaMemoryTypeDevice = 2 cudaMemoryTypeManaged = 3 cdef enum cudaMemcpyKind: cudaMemcpyHostToHost = 0 cudaMemcpyHostToDevice = 1 cudaMemcpyDeviceToHost = 2 cudaMemcpyDeviceToDevice = 3 cudaMemcpyDefault = 4 cdef enum cudaAccessProperty: cudaAccessPropertyNormal = 0 cudaAccessPropertyStreaming = 1 cudaAccessPropertyPersisting = 2 cdef enum cudaStreamCaptureStatus: cudaStreamCaptureStatusNone = 0 cudaStreamCaptureStatusActive = 1 cudaStreamCaptureStatusInvalidated = 2 cdef enum cudaStreamCaptureMode: cudaStreamCaptureModeGlobal = 0 cudaStreamCaptureModeThreadLocal = 1 cudaStreamCaptureModeRelaxed = 2 cdef enum cudaSynchronizationPolicy: cudaSyncPolicyAuto = 1 cudaSyncPolicySpin = 2 cudaSyncPolicyYield = 3 cudaSyncPolicyBlockingSync = 4 cdef enum cudaClusterSchedulingPolicy: cudaClusterSchedulingPolicyDefault = 0 cudaClusterSchedulingPolicySpread = 1 cudaClusterSchedulingPolicyLoadBalancing = 2 cdef enum cudaStreamUpdateCaptureDependenciesFlags: cudaStreamAddCaptureDependencies = 0 cudaStreamSetCaptureDependencies = 1 cdef enum cudaUserObjectFlags: cudaUserObjectNoDestructorSync = 1 cdef enum cudaUserObjectRetainFlags: cudaGraphUserObjectMove = 1 cdef enum cudaGraphicsRegisterFlags: cudaGraphicsRegisterFlagsNone = 0 cudaGraphicsRegisterFlagsReadOnly = 1 cudaGraphicsRegisterFlagsWriteDiscard = 2 cudaGraphicsRegisterFlagsSurfaceLoadStore = 4 cudaGraphicsRegisterFlagsTextureGather = 8 cdef enum cudaGraphicsMapFlags: cudaGraphicsMapFlagsNone = 0 cudaGraphicsMapFlagsReadOnly = 1 cudaGraphicsMapFlagsWriteDiscard = 2 cdef enum cudaGraphicsCubeFace: cudaGraphicsCubeFacePositiveX = 0 cudaGraphicsCubeFaceNegativeX = 1 cudaGraphicsCubeFacePositiveY = 2 cudaGraphicsCubeFaceNegativeY = 3 cudaGraphicsCubeFacePositiveZ = 4 cudaGraphicsCubeFaceNegativeZ = 5 cdef enum cudaResourceType: cudaResourceTypeArray = 0 cudaResourceTypeMipmappedArray = 1 cudaResourceTypeLinear = 2 cudaResourceTypePitch2D = 3 cdef enum cudaResourceViewFormat: cudaResViewFormatNone = 0 cudaResViewFormatUnsignedChar1 = 1 cudaResViewFormatUnsignedChar2 = 2 cudaResViewFormatUnsignedChar4 = 3 cudaResViewFormatSignedChar1 = 4 cudaResViewFormatSignedChar2 = 5 cudaResViewFormatSignedChar4 = 6 cudaResViewFormatUnsignedShort1 = 7 cudaResViewFormatUnsignedShort2 = 8 cudaResViewFormatUnsignedShort4 = 9 cudaResViewFormatSignedShort1 = 10 cudaResViewFormatSignedShort2 = 11 cudaResViewFormatSignedShort4 = 12 cudaResViewFormatUnsignedInt1 = 13 cudaResViewFormatUnsignedInt2 = 14 cudaResViewFormatUnsignedInt4 = 15 cudaResViewFormatSignedInt1 = 16 cudaResViewFormatSignedInt2 = 17 cudaResViewFormatSignedInt4 = 18 cudaResViewFormatHalf1 = 19 cudaResViewFormatHalf2 = 20 cudaResViewFormatHalf4 = 21 cudaResViewFormatFloat1 = 22 cudaResViewFormatFloat2 = 23 cudaResViewFormatFloat4 = 24 cudaResViewFormatUnsignedBlockCompressed1 = 25 cudaResViewFormatUnsignedBlockCompressed2 = 26 cudaResViewFormatUnsignedBlockCompressed3 = 27 cudaResViewFormatUnsignedBlockCompressed4 = 28 cudaResViewFormatSignedBlockCompressed4 = 29 cudaResViewFormatUnsignedBlockCompressed5 = 30 cudaResViewFormatSignedBlockCompressed5 = 31 cudaResViewFormatUnsignedBlockCompressed6H = 32 cudaResViewFormatSignedBlockCompressed6H = 33 cudaResViewFormatUnsignedBlockCompressed7 = 34 cdef enum cudaFuncAttribute: cudaFuncAttributeMaxDynamicSharedMemorySize = 8 cudaFuncAttributePreferredSharedMemoryCarveout = 9 cudaFuncAttributeClusterDimMustBeSet = 10 cudaFuncAttributeRequiredClusterWidth = 11 cudaFuncAttributeRequiredClusterHeight = 12 cudaFuncAttributeRequiredClusterDepth = 13 cudaFuncAttributeNonPortableClusterSizeAllowed = 14 cudaFuncAttributeClusterSchedulingPolicyPreference = 15 cudaFuncAttributeMax = 16 cdef enum cudaFuncCache: cudaFuncCachePreferNone = 0 cudaFuncCachePreferShared = 1 cudaFuncCachePreferL1 = 2 cudaFuncCachePreferEqual = 3 cdef enum cudaSharedMemConfig: cudaSharedMemBankSizeDefault = 0 cudaSharedMemBankSizeFourByte = 1 cudaSharedMemBankSizeEightByte = 2 cdef enum cudaSharedCarveout: cudaSharedmemCarveoutDefault = -1 cudaSharedmemCarveoutMaxL1 = 0 cudaSharedmemCarveoutMaxShared = 100 cdef enum cudaComputeMode: cudaComputeModeDefault = 0 cudaComputeModeExclusive = 1 cudaComputeModeProhibited = 2 cudaComputeModeExclusiveProcess = 3 cdef enum cudaLimit: cudaLimitStackSize = 0 cudaLimitPrintfFifoSize = 1 cudaLimitMallocHeapSize = 2 cudaLimitDevRuntimeSyncDepth = 3 cudaLimitDevRuntimePendingLaunchCount = 4 cudaLimitMaxL2FetchGranularity = 5 cudaLimitPersistingL2CacheSize = 6 cdef enum cudaMemoryAdvise: cudaMemAdviseSetReadMostly = 1 cudaMemAdviseUnsetReadMostly = 2 cudaMemAdviseSetPreferredLocation = 3 cudaMemAdviseUnsetPreferredLocation = 4 cudaMemAdviseSetAccessedBy = 5 cudaMemAdviseUnsetAccessedBy = 6 cdef enum cudaMemRangeAttribute: cudaMemRangeAttributeReadMostly = 1 cudaMemRangeAttributePreferredLocation = 2 cudaMemRangeAttributeAccessedBy = 3 cudaMemRangeAttributeLastPrefetchLocation = 4 cudaMemRangeAttributePreferredLocationType = 5 cudaMemRangeAttributePreferredLocationId = 6 cudaMemRangeAttributeLastPrefetchLocationType = 7 cudaMemRangeAttributeLastPrefetchLocationId = 8 cdef enum cudaFlushGPUDirectRDMAWritesOptions: cudaFlushGPUDirectRDMAWritesOptionHost = 1 cudaFlushGPUDirectRDMAWritesOptionMemOps = 2 cdef enum cudaGPUDirectRDMAWritesOrdering: cudaGPUDirectRDMAWritesOrderingNone = 0 cudaGPUDirectRDMAWritesOrderingOwner = 100 cudaGPUDirectRDMAWritesOrderingAllDevices = 200 cdef enum cudaFlushGPUDirectRDMAWritesScope: cudaFlushGPUDirectRDMAWritesToOwner = 100 cudaFlushGPUDirectRDMAWritesToAllDevices = 200 cdef enum cudaFlushGPUDirectRDMAWritesTarget: cudaFlushGPUDirectRDMAWritesTargetCurrentDevice = 0 cdef enum cudaDeviceAttr: cudaDevAttrMaxThreadsPerBlock = 1 cudaDevAttrMaxBlockDimX = 2 cudaDevAttrMaxBlockDimY = 3 cudaDevAttrMaxBlockDimZ = 4 cudaDevAttrMaxGridDimX = 5 cudaDevAttrMaxGridDimY = 6 cudaDevAttrMaxGridDimZ = 7 cudaDevAttrMaxSharedMemoryPerBlock = 8 cudaDevAttrTotalConstantMemory = 9 cudaDevAttrWarpSize = 10 cudaDevAttrMaxPitch = 11 cudaDevAttrMaxRegistersPerBlock = 12 cudaDevAttrClockRate = 13 cudaDevAttrTextureAlignment = 14 cudaDevAttrGpuOverlap = 15 cudaDevAttrMultiProcessorCount = 16 cudaDevAttrKernelExecTimeout = 17 cudaDevAttrIntegrated = 18 cudaDevAttrCanMapHostMemory = 19 cudaDevAttrComputeMode = 20 cudaDevAttrMaxTexture1DWidth = 21 cudaDevAttrMaxTexture2DWidth = 22 cudaDevAttrMaxTexture2DHeight = 23 cudaDevAttrMaxTexture3DWidth = 24 cudaDevAttrMaxTexture3DHeight = 25 cudaDevAttrMaxTexture3DDepth = 26 cudaDevAttrMaxTexture2DLayeredWidth = 27 cudaDevAttrMaxTexture2DLayeredHeight = 28 cudaDevAttrMaxTexture2DLayeredLayers = 29 cudaDevAttrSurfaceAlignment = 30 cudaDevAttrConcurrentKernels = 31 cudaDevAttrEccEnabled = 32 cudaDevAttrPciBusId = 33 cudaDevAttrPciDeviceId = 34 cudaDevAttrTccDriver = 35 cudaDevAttrMemoryClockRate = 36 cudaDevAttrGlobalMemoryBusWidth = 37 cudaDevAttrL2CacheSize = 38 cudaDevAttrMaxThreadsPerMultiProcessor = 39 cudaDevAttrAsyncEngineCount = 40 cudaDevAttrUnifiedAddressing = 41 cudaDevAttrMaxTexture1DLayeredWidth = 42 cudaDevAttrMaxTexture1DLayeredLayers = 43 cudaDevAttrMaxTexture2DGatherWidth = 45 cudaDevAttrMaxTexture2DGatherHeight = 46 cudaDevAttrMaxTexture3DWidthAlt = 47 cudaDevAttrMaxTexture3DHeightAlt = 48 cudaDevAttrMaxTexture3DDepthAlt = 49 cudaDevAttrPciDomainId = 50 cudaDevAttrTexturePitchAlignment = 51 cudaDevAttrMaxTextureCubemapWidth = 52 cudaDevAttrMaxTextureCubemapLayeredWidth = 53 cudaDevAttrMaxTextureCubemapLayeredLayers = 54 cudaDevAttrMaxSurface1DWidth = 55 cudaDevAttrMaxSurface2DWidth = 56 cudaDevAttrMaxSurface2DHeight = 57 cudaDevAttrMaxSurface3DWidth = 58 cudaDevAttrMaxSurface3DHeight = 59 cudaDevAttrMaxSurface3DDepth = 60 cudaDevAttrMaxSurface1DLayeredWidth = 61 cudaDevAttrMaxSurface1DLayeredLayers = 62 cudaDevAttrMaxSurface2DLayeredWidth = 63 cudaDevAttrMaxSurface2DLayeredHeight = 64 cudaDevAttrMaxSurface2DLayeredLayers = 65 cudaDevAttrMaxSurfaceCubemapWidth = 66 cudaDevAttrMaxSurfaceCubemapLayeredWidth = 67 cudaDevAttrMaxSurfaceCubemapLayeredLayers = 68 cudaDevAttrMaxTexture1DLinearWidth = 69 cudaDevAttrMaxTexture2DLinearWidth = 70 cudaDevAttrMaxTexture2DLinearHeight = 71 cudaDevAttrMaxTexture2DLinearPitch = 72 cudaDevAttrMaxTexture2DMipmappedWidth = 73 cudaDevAttrMaxTexture2DMipmappedHeight = 74 cudaDevAttrComputeCapabilityMajor = 75 cudaDevAttrComputeCapabilityMinor = 76 cudaDevAttrMaxTexture1DMipmappedWidth = 77 cudaDevAttrStreamPrioritiesSupported = 78 cudaDevAttrGlobalL1CacheSupported = 79 cudaDevAttrLocalL1CacheSupported = 80 cudaDevAttrMaxSharedMemoryPerMultiprocessor = 81 cudaDevAttrMaxRegistersPerMultiprocessor = 82 cudaDevAttrManagedMemory = 83 cudaDevAttrIsMultiGpuBoard = 84 cudaDevAttrMultiGpuBoardGroupID = 85 cudaDevAttrHostNativeAtomicSupported = 86 cudaDevAttrSingleToDoublePrecisionPerfRatio = 87 cudaDevAttrPageableMemoryAccess = 88 cudaDevAttrConcurrentManagedAccess = 89 cudaDevAttrComputePreemptionSupported = 90 cudaDevAttrCanUseHostPointerForRegisteredMem = 91 cudaDevAttrReserved92 = 92 cudaDevAttrReserved93 = 93 cudaDevAttrReserved94 = 94 cudaDevAttrCooperativeLaunch = 95 cudaDevAttrCooperativeMultiDeviceLaunch = 96 cudaDevAttrMaxSharedMemoryPerBlockOptin = 97 cudaDevAttrCanFlushRemoteWrites = 98 cudaDevAttrHostRegisterSupported = 99 cudaDevAttrPageableMemoryAccessUsesHostPageTables = 100 cudaDevAttrDirectManagedMemAccessFromHost = 101 cudaDevAttrMaxBlocksPerMultiprocessor = 106 cudaDevAttrMaxPersistingL2CacheSize = 108 cudaDevAttrMaxAccessPolicyWindowSize = 109 cudaDevAttrReservedSharedMemoryPerBlock = 111 cudaDevAttrSparseCudaArraySupported = 112 cudaDevAttrHostRegisterReadOnlySupported = 113 cudaDevAttrTimelineSemaphoreInteropSupported = 114 cudaDevAttrMaxTimelineSemaphoreInteropSupported = 114 cudaDevAttrMemoryPoolsSupported = 115 cudaDevAttrGPUDirectRDMASupported = 116 cudaDevAttrGPUDirectRDMAFlushWritesOptions = 117 cudaDevAttrGPUDirectRDMAWritesOrdering = 118 cudaDevAttrMemoryPoolSupportedHandleTypes = 119 cudaDevAttrClusterLaunch = 120 cudaDevAttrDeferredMappingCudaArraySupported = 121 cudaDevAttrReserved122 = 122 cudaDevAttrReserved123 = 123 cudaDevAttrReserved124 = 124 cudaDevAttrIpcEventSupport = 125 cudaDevAttrMemSyncDomainCount = 126 cudaDevAttrReserved127 = 127 cudaDevAttrReserved128 = 128 cudaDevAttrReserved129 = 129 cudaDevAttrNumaConfig = 130 cudaDevAttrNumaId = 131 cudaDevAttrReserved132 = 132 cudaDevAttrMpsEnabled = 133 cudaDevAttrHostNumaId = 134 cudaDevAttrD3D12CigSupported = 135 cudaDevAttrMax = 136 cdef enum cudaMemPoolAttr: cudaMemPoolReuseFollowEventDependencies = 1 cudaMemPoolReuseAllowOpportunistic = 2 cudaMemPoolReuseAllowInternalDependencies = 3 cudaMemPoolAttrReleaseThreshold = 4 cudaMemPoolAttrReservedMemCurrent = 5 cudaMemPoolAttrReservedMemHigh = 6 cudaMemPoolAttrUsedMemCurrent = 7 cudaMemPoolAttrUsedMemHigh = 8 cdef enum cudaMemLocationType: cudaMemLocationTypeInvalid = 0 cudaMemLocationTypeDevice = 1 cudaMemLocationTypeHost = 2 cudaMemLocationTypeHostNuma = 3 cudaMemLocationTypeHostNumaCurrent = 4 cdef enum cudaMemAccessFlags: cudaMemAccessFlagsProtNone = 0 cudaMemAccessFlagsProtRead = 1 cudaMemAccessFlagsProtReadWrite = 3 cdef enum cudaMemAllocationType: cudaMemAllocationTypeInvalid = 0 cudaMemAllocationTypePinned = 1 cudaMemAllocationTypeMax = 2147483647 cdef enum cudaMemAllocationHandleType: cudaMemHandleTypeNone = 0 cudaMemHandleTypePosixFileDescriptor = 1 cudaMemHandleTypeWin32 = 2 cudaMemHandleTypeWin32Kmt = 4 cudaMemHandleTypeFabric = 8 cdef enum cudaGraphMemAttributeType: cudaGraphMemAttrUsedMemCurrent = 0 cudaGraphMemAttrUsedMemHigh = 1 cudaGraphMemAttrReservedMemCurrent = 2 cudaGraphMemAttrReservedMemHigh = 3 cdef enum cudaDeviceP2PAttr: cudaDevP2PAttrPerformanceRank = 1 cudaDevP2PAttrAccessSupported = 2 cudaDevP2PAttrNativeAtomicSupported = 3 cudaDevP2PAttrCudaArrayAccessSupported = 4 cdef enum cudaExternalMemoryHandleType: cudaExternalMemoryHandleTypeOpaqueFd = 1 cudaExternalMemoryHandleTypeOpaqueWin32 = 2 cudaExternalMemoryHandleTypeOpaqueWin32Kmt = 3 cudaExternalMemoryHandleTypeD3D12Heap = 4 cudaExternalMemoryHandleTypeD3D12Resource = 5 cudaExternalMemoryHandleTypeD3D11Resource = 6 cudaExternalMemoryHandleTypeD3D11ResourceKmt = 7 cudaExternalMemoryHandleTypeNvSciBuf = 8 cdef enum cudaExternalSemaphoreHandleType: cudaExternalSemaphoreHandleTypeOpaqueFd = 1 cudaExternalSemaphoreHandleTypeOpaqueWin32 = 2 cudaExternalSemaphoreHandleTypeOpaqueWin32Kmt = 3 cudaExternalSemaphoreHandleTypeD3D12Fence = 4 cudaExternalSemaphoreHandleTypeD3D11Fence = 5 cudaExternalSemaphoreHandleTypeNvSciSync = 6 cudaExternalSemaphoreHandleTypeKeyedMutex = 7 cudaExternalSemaphoreHandleTypeKeyedMutexKmt = 8 cudaExternalSemaphoreHandleTypeTimelineSemaphoreFd = 9 cudaExternalSemaphoreHandleTypeTimelineSemaphoreWin32 = 10 cdef enum cudaCGScope: cudaCGScopeInvalid = 0 cudaCGScopeGrid = 1 cudaCGScopeMultiGrid = 2 cdef enum cudaGraphConditionalHandleFlags: cudaGraphCondAssignDefault = 1 cdef enum cudaGraphConditionalNodeType: cudaGraphCondTypeIf = 0 cudaGraphCondTypeWhile = 1 cdef enum cudaGraphNodeType: cudaGraphNodeTypeKernel = 0 cudaGraphNodeTypeMemcpy = 1 cudaGraphNodeTypeMemset = 2 cudaGraphNodeTypeHost = 3 cudaGraphNodeTypeGraph = 4 cudaGraphNodeTypeEmpty = 5 cudaGraphNodeTypeWaitEvent = 6 cudaGraphNodeTypeEventRecord = 7 cudaGraphNodeTypeExtSemaphoreSignal = 8 cudaGraphNodeTypeExtSemaphoreWait = 9 cudaGraphNodeTypeMemAlloc = 10 cudaGraphNodeTypeMemFree = 11 cudaGraphNodeTypeConditional = 13 cudaGraphNodeTypeCount = 14 cdef enum cudaGraphExecUpdateResult: cudaGraphExecUpdateSuccess = 0 cudaGraphExecUpdateError = 1 cudaGraphExecUpdateErrorTopologyChanged = 2 cudaGraphExecUpdateErrorNodeTypeChanged = 3 cudaGraphExecUpdateErrorFunctionChanged = 4 cudaGraphExecUpdateErrorParametersChanged = 5 cudaGraphExecUpdateErrorNotSupported = 6 cudaGraphExecUpdateErrorUnsupportedFunctionChange = 7 cudaGraphExecUpdateErrorAttributesChanged = 8 cdef enum cudaGraphKernelNodeField: cudaGraphKernelNodeFieldInvalid = 0 cudaGraphKernelNodeFieldGridDim = 1 cudaGraphKernelNodeFieldParam = 2 cudaGraphKernelNodeFieldEnabled = 3 cdef enum cudaGetDriverEntryPointFlags: cudaEnableDefault = 0 cudaEnableLegacyStream = 1 cudaEnablePerThreadDefaultStream = 2 cdef enum cudaDriverEntryPointQueryResult: cudaDriverEntryPointSuccess = 0 cudaDriverEntryPointSymbolNotFound = 1 cudaDriverEntryPointVersionNotSufficent = 2 cdef enum cudaGraphDebugDotFlags: cudaGraphDebugDotFlagsVerbose = 1 cudaGraphDebugDotFlagsKernelNodeParams = 4 cudaGraphDebugDotFlagsMemcpyNodeParams = 8 cudaGraphDebugDotFlagsMemsetNodeParams = 16 cudaGraphDebugDotFlagsHostNodeParams = 32 cudaGraphDebugDotFlagsEventNodeParams = 64 cudaGraphDebugDotFlagsExtSemasSignalNodeParams = 128 cudaGraphDebugDotFlagsExtSemasWaitNodeParams = 256 cudaGraphDebugDotFlagsKernelNodeAttributes = 512 cudaGraphDebugDotFlagsHandles = 1024 cudaGraphDebugDotFlagsConditionalNodeParams = 32768 cdef enum cudaGraphInstantiateFlags: cudaGraphInstantiateFlagAutoFreeOnLaunch = 1 cudaGraphInstantiateFlagUpload = 2 cudaGraphInstantiateFlagDeviceLaunch = 4 cudaGraphInstantiateFlagUseNodePriority = 8 cdef enum cudaDeviceNumaConfig: cudaDeviceNumaConfigNone = 0 cudaDeviceNumaConfigNumaNode = 1 cdef extern from "surface_types.h": ctypedef unsigned long long cudaSurfaceObject_t cdef enum cudaSurfaceBoundaryMode: cudaBoundaryModeZero = 0 cudaBoundaryModeClamp = 1 cudaBoundaryModeTrap = 2 cdef enum cudaSurfaceFormatMode: cudaFormatModeForced = 0 cudaFormatModeAuto = 1 cdef extern from "texture_types.h": cdef struct cudaTextureDesc: cudaTextureAddressMode addressMode[3] cudaTextureFilterMode filterMode cudaTextureReadMode readMode int sRGB float borderColor[4] int normalizedCoords unsigned int maxAnisotropy cudaTextureFilterMode mipmapFilterMode float mipmapLevelBias float minMipmapLevelClamp float maxMipmapLevelClamp int disableTrilinearOptimization int seamlessCubemap ctypedef unsigned long long cudaTextureObject_t cdef enum cudaTextureAddressMode: cudaAddressModeWrap = 0 cudaAddressModeClamp = 1 cudaAddressModeMirror = 2 cudaAddressModeBorder = 3 cdef enum cudaTextureFilterMode: cudaFilterModePoint = 0 cudaFilterModeLinear = 1 cdef enum cudaTextureReadMode: cudaReadModeElementType = 0 cudaReadModeNormalizedFloat = 1 cdef extern from "library_types.h": cdef enum cudaDataType_t: CUDA_R_32F = 0 CUDA_R_64F = 1 CUDA_R_16F = 2 CUDA_R_8I = 3 CUDA_C_32F = 4 CUDA_C_64F = 5 CUDA_C_16F = 6 CUDA_C_8I = 7 CUDA_R_8U = 8 CUDA_C_8U = 9 CUDA_R_32I = 10 CUDA_C_32I = 11 CUDA_R_32U = 12 CUDA_C_32U = 13 CUDA_R_16BF = 14 CUDA_C_16BF = 15 CUDA_R_4I = 16 CUDA_C_4I = 17 CUDA_R_4U = 18 CUDA_C_4U = 19 CUDA_R_16I = 20 CUDA_C_16I = 21 CUDA_R_16U = 22 CUDA_C_16U = 23 CUDA_R_64I = 24 CUDA_C_64I = 25 CUDA_R_64U = 26 CUDA_C_64U = 27 CUDA_R_8F_E4M3 = 28 CUDA_R_8F_E5M2 = 29 ctypedef cudaDataType_t cudaDataType cdef enum libraryPropertyType_t: MAJOR_VERSION = 0 MINOR_VERSION = 1 PATCH_LEVEL = 2 ctypedef libraryPropertyType_t libraryPropertyType cdef extern from "cuda_runtime_api.h": ctypedef void (*cudaStreamCallback_t)(cudaStream_t stream, cudaError_t status, void* userData) cdef extern from "device_types.h": cdef enum cudaRoundMode: cudaRoundNearest = 0 cudaRoundZero = 1 cudaRoundPosInf = 2 cudaRoundMinInf = 3 ctypedef unsigned int GLenum ctypedef unsigned int GLuint cdef extern from "": cdef struct void: pass ctypedef void* EGLImageKHR cdef extern from "": cdef struct void: pass ctypedef void* EGLStreamKHR ctypedef unsigned int EGLint cdef extern from "": cdef struct void: pass ctypedef void* EGLSyncKHR ctypedef uint32_t VdpDevice ctypedef unsigned long long VdpGetProcAddress ctypedef uint32_t VdpVideoSurface ctypedef uint32_t VdpOutputSurface ctypedef cudaLaunchAttributeID cudaStreamAttrID ctypedef cudaLaunchAttributeID cudaKernelNodeAttrID ctypedef cudaLaunchAttributeValue cudaStreamAttrValue ctypedef cudaLaunchAttributeValue cudaKernelNodeAttrValue cdef enum cudaEglFrameType_enum: cudaEglFrameTypeArray = 0 cudaEglFrameTypePitch = 1 ctypedef cudaEglFrameType_enum cudaEglFrameType cdef enum cudaEglResourceLocationFlags_enum: cudaEglResourceLocationSysmem = 0 cudaEglResourceLocationVidmem = 1 ctypedef cudaEglResourceLocationFlags_enum cudaEglResourceLocationFlags cdef enum cudaEglColorFormat_enum: cudaEglColorFormatYUV420Planar = 0 cudaEglColorFormatYUV420SemiPlanar = 1 cudaEglColorFormatYUV422Planar = 2 cudaEglColorFormatYUV422SemiPlanar = 3 cudaEglColorFormatARGB = 6 cudaEglColorFormatRGBA = 7 cudaEglColorFormatL = 8 cudaEglColorFormatR = 9 cudaEglColorFormatYUV444Planar = 10 cudaEglColorFormatYUV444SemiPlanar = 11 cudaEglColorFormatYUYV422 = 12 cudaEglColorFormatUYVY422 = 13 cudaEglColorFormatABGR = 14 cudaEglColorFormatBGRA = 15 cudaEglColorFormatA = 16 cudaEglColorFormatRG = 17 cudaEglColorFormatAYUV = 18 cudaEglColorFormatYVU444SemiPlanar = 19 cudaEglColorFormatYVU422SemiPlanar = 20 cudaEglColorFormatYVU420SemiPlanar = 21 cudaEglColorFormatY10V10U10_444SemiPlanar = 22 cudaEglColorFormatY10V10U10_420SemiPlanar = 23 cudaEglColorFormatY12V12U12_444SemiPlanar = 24 cudaEglColorFormatY12V12U12_420SemiPlanar = 25 cudaEglColorFormatVYUY_ER = 26 cudaEglColorFormatUYVY_ER = 27 cudaEglColorFormatYUYV_ER = 28 cudaEglColorFormatYVYU_ER = 29 cudaEglColorFormatYUVA_ER = 31 cudaEglColorFormatAYUV_ER = 32 cudaEglColorFormatYUV444Planar_ER = 33 cudaEglColorFormatYUV422Planar_ER = 34 cudaEglColorFormatYUV420Planar_ER = 35 cudaEglColorFormatYUV444SemiPlanar_ER = 36 cudaEglColorFormatYUV422SemiPlanar_ER = 37 cudaEglColorFormatYUV420SemiPlanar_ER = 38 cudaEglColorFormatYVU444Planar_ER = 39 cudaEglColorFormatYVU422Planar_ER = 40 cudaEglColorFormatYVU420Planar_ER = 41 cudaEglColorFormatYVU444SemiPlanar_ER = 42 cudaEglColorFormatYVU422SemiPlanar_ER = 43 cudaEglColorFormatYVU420SemiPlanar_ER = 44 cudaEglColorFormatBayerRGGB = 45 cudaEglColorFormatBayerBGGR = 46 cudaEglColorFormatBayerGRBG = 47 cudaEglColorFormatBayerGBRG = 48 cudaEglColorFormatBayer10RGGB = 49 cudaEglColorFormatBayer10BGGR = 50 cudaEglColorFormatBayer10GRBG = 51 cudaEglColorFormatBayer10GBRG = 52 cudaEglColorFormatBayer12RGGB = 53 cudaEglColorFormatBayer12BGGR = 54 cudaEglColorFormatBayer12GRBG = 55 cudaEglColorFormatBayer12GBRG = 56 cudaEglColorFormatBayer14RGGB = 57 cudaEglColorFormatBayer14BGGR = 58 cudaEglColorFormatBayer14GRBG = 59 cudaEglColorFormatBayer14GBRG = 60 cudaEglColorFormatBayer20RGGB = 61 cudaEglColorFormatBayer20BGGR = 62 cudaEglColorFormatBayer20GRBG = 63 cudaEglColorFormatBayer20GBRG = 64 cudaEglColorFormatYVU444Planar = 65 cudaEglColorFormatYVU422Planar = 66 cudaEglColorFormatYVU420Planar = 67 cudaEglColorFormatBayerIspRGGB = 68 cudaEglColorFormatBayerIspBGGR = 69 cudaEglColorFormatBayerIspGRBG = 70 cudaEglColorFormatBayerIspGBRG = 71 cudaEglColorFormatBayerBCCR = 72 cudaEglColorFormatBayerRCCB = 73 cudaEglColorFormatBayerCRBC = 74 cudaEglColorFormatBayerCBRC = 75 cudaEglColorFormatBayer10CCCC = 76 cudaEglColorFormatBayer12BCCR = 77 cudaEglColorFormatBayer12RCCB = 78 cudaEglColorFormatBayer12CRBC = 79 cudaEglColorFormatBayer12CBRC = 80 cudaEglColorFormatBayer12CCCC = 81 cudaEglColorFormatY = 82 cudaEglColorFormatYUV420SemiPlanar_2020 = 83 cudaEglColorFormatYVU420SemiPlanar_2020 = 84 cudaEglColorFormatYUV420Planar_2020 = 85 cudaEglColorFormatYVU420Planar_2020 = 86 cudaEglColorFormatYUV420SemiPlanar_709 = 87 cudaEglColorFormatYVU420SemiPlanar_709 = 88 cudaEglColorFormatYUV420Planar_709 = 89 cudaEglColorFormatYVU420Planar_709 = 90 cudaEglColorFormatY10V10U10_420SemiPlanar_709 = 91 cudaEglColorFormatY10V10U10_420SemiPlanar_2020 = 92 cudaEglColorFormatY10V10U10_422SemiPlanar_2020 = 93 cudaEglColorFormatY10V10U10_422SemiPlanar = 94 cudaEglColorFormatY10V10U10_422SemiPlanar_709 = 95 cudaEglColorFormatY_ER = 96 cudaEglColorFormatY_709_ER = 97 cudaEglColorFormatY10_ER = 98 cudaEglColorFormatY10_709_ER = 99 cudaEglColorFormatY12_ER = 100 cudaEglColorFormatY12_709_ER = 101 cudaEglColorFormatYUVA = 102 cudaEglColorFormatYVYU = 104 cudaEglColorFormatVYUY = 105 cudaEglColorFormatY10V10U10_420SemiPlanar_ER = 106 cudaEglColorFormatY10V10U10_420SemiPlanar_709_ER = 107 cudaEglColorFormatY10V10U10_444SemiPlanar_ER = 108 cudaEglColorFormatY10V10U10_444SemiPlanar_709_ER = 109 cudaEglColorFormatY12V12U12_420SemiPlanar_ER = 110 cudaEglColorFormatY12V12U12_420SemiPlanar_709_ER = 111 cudaEglColorFormatY12V12U12_444SemiPlanar_ER = 112 cudaEglColorFormatY12V12U12_444SemiPlanar_709_ER = 113 ctypedef cudaEglColorFormat_enum cudaEglColorFormat cdef struct cudaEglPlaneDesc_st: unsigned int width unsigned int height unsigned int depth unsigned int pitch unsigned int numChannels cudaChannelFormatDesc channelDesc unsigned int reserved[4] ctypedef cudaEglPlaneDesc_st cudaEglPlaneDesc cdef union anon_union10: cudaArray_t pArray[3] cudaPitchedPtr pPitch[3] cdef struct cudaEglFrame_st: anon_union10 frame cudaEglPlaneDesc planeDesc[3] unsigned int planeCount cudaEglFrameType frameType cudaEglColorFormat eglColorFormat ctypedef cudaEglFrame_st cudaEglFrame cdef extern from "": cdef struct CUeglStreamConnection_st: pass ctypedef CUeglStreamConnection_st* cudaEglStreamConnection cdef enum cudaGLDeviceList: cudaGLDeviceListAll = 1 cudaGLDeviceListCurrentFrame = 2 cudaGLDeviceListNextFrame = 3 cdef enum cudaGLMapFlags: cudaGLMapFlagsNone = 0 cudaGLMapFlagsReadOnly = 1 cudaGLMapFlagsWriteDiscard = 2 cdef cudaError_t cudaDeviceReset() except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceSynchronize() except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceSetLimit(cudaLimit limit, size_t value) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetLimit(size_t* pValue, cudaLimit limit) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetTexture1DLinearMaxWidth(size_t* maxWidthInElements, const cudaChannelFormatDesc* fmtDesc, int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetCacheConfig(cudaFuncCache* pCacheConfig) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetStreamPriorityRange(int* leastPriority, int* greatestPriority) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceSetCacheConfig(cudaFuncCache cacheConfig) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetByPCIBusId(int* device, const char* pciBusId) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetPCIBusId(char* pciBusId, int length, int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaIpcGetEventHandle(cudaIpcEventHandle_t* handle, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaIpcOpenEventHandle(cudaEvent_t* event, cudaIpcEventHandle_t handle) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaIpcGetMemHandle(cudaIpcMemHandle_t* handle, void* devPtr) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaIpcOpenMemHandle(void** devPtr, cudaIpcMemHandle_t handle, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaIpcCloseMemHandle(void* devPtr) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceFlushGPUDirectRDMAWrites(cudaFlushGPUDirectRDMAWritesTarget target, cudaFlushGPUDirectRDMAWritesScope scope) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceRegisterAsyncNotification(int device, cudaAsyncCallback callbackFunc, void* userData, cudaAsyncCallbackHandle_t* callback) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceUnregisterAsyncNotification(int device, cudaAsyncCallbackHandle_t callback) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetSharedMemConfig(cudaSharedMemConfig* pConfig) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceSetSharedMemConfig(cudaSharedMemConfig config) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetLastError() except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaPeekAtLastError() except ?cudaErrorCallRequiresNewerDriver nogil cdef const char* cudaGetErrorName(cudaError_t error) except ?NULL nogil cdef const char* cudaGetErrorString(cudaError_t error) except ?NULL nogil cdef cudaError_t cudaGetDeviceCount(int* count) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetDeviceProperties(cudaDeviceProp* prop, int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetAttribute(int* value, cudaDeviceAttr attr, int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetDefaultMemPool(cudaMemPool_t* memPool, int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceSetMemPool(int device, cudaMemPool_t memPool) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetMemPool(cudaMemPool_t* memPool, int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, int device, int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetP2PAttribute(int* value, cudaDeviceP2PAttr attr, int srcDevice, int dstDevice) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaChooseDevice(int* device, const cudaDeviceProp* prop) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaInitDevice(int device, unsigned int deviceFlags, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaSetDevice(int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetDevice(int* device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaSetDeviceFlags(unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetDeviceFlags(unsigned int* flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamCreate(cudaStream_t* pStream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamCreateWithFlags(cudaStream_t* pStream, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamCreateWithPriority(cudaStream_t* pStream, unsigned int flags, int priority) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamGetPriority(cudaStream_t hStream, int* priority) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamGetFlags(cudaStream_t hStream, unsigned int* flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamGetId(cudaStream_t hStream, unsigned long long* streamId) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaCtxResetPersistingL2Cache() except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamCopyAttributes(cudaStream_t dst, cudaStream_t src) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamGetAttribute(cudaStream_t hStream, cudaStreamAttrID attr, cudaStreamAttrValue* value_out) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamSetAttribute(cudaStream_t hStream, cudaStreamAttrID attr, const cudaStreamAttrValue* value) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamDestroy(cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamWaitEvent(cudaStream_t stream, cudaEvent_t event, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamAddCallback(cudaStream_t stream, cudaStreamCallback_t callback, void* userData, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamSynchronize(cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamQuery(cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamAttachMemAsync(cudaStream_t stream, void* devPtr, size_t length, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamBeginCapture(cudaStream_t stream, cudaStreamCaptureMode mode) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamBeginCaptureToGraph(cudaStream_t stream, cudaGraph_t graph, const cudaGraphNode_t* dependencies, const cudaGraphEdgeData* dependencyData, size_t numDependencies, cudaStreamCaptureMode mode) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaThreadExchangeStreamCaptureMode(cudaStreamCaptureMode* mode) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamEndCapture(cudaStream_t stream, cudaGraph_t* pGraph) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamIsCapturing(cudaStream_t stream, cudaStreamCaptureStatus* pCaptureStatus) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamGetCaptureInfo(cudaStream_t stream, cudaStreamCaptureStatus* captureStatus_out, unsigned long long* id_out, cudaGraph_t* graph_out, const cudaGraphNode_t** dependencies_out, size_t* numDependencies_out) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamGetCaptureInfo_v3(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 cdef cudaError_t cudaStreamUpdateCaptureDependencies(cudaStream_t stream, cudaGraphNode_t* dependencies, size_t numDependencies, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaStreamUpdateCaptureDependencies_v2(cudaStream_t stream, cudaGraphNode_t* dependencies, const cudaGraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEventCreate(cudaEvent_t* event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEventCreateWithFlags(cudaEvent_t* event, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEventRecord(cudaEvent_t event, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEventRecordWithFlags(cudaEvent_t event, cudaStream_t stream, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEventQuery(cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEventSynchronize(cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEventDestroy(cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEventElapsedTime(float* ms, cudaEvent_t start, cudaEvent_t end) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaImportExternalMemory(cudaExternalMemory_t* extMem_out, const cudaExternalMemoryHandleDesc* memHandleDesc) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaExternalMemoryGetMappedBuffer(void** devPtr, cudaExternalMemory_t extMem, const cudaExternalMemoryBufferDesc* bufferDesc) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaExternalMemoryGetMappedMipmappedArray(cudaMipmappedArray_t* mipmap, cudaExternalMemory_t extMem, const cudaExternalMemoryMipmappedArrayDesc* mipmapDesc) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDestroyExternalMemory(cudaExternalMemory_t extMem) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaImportExternalSemaphore(cudaExternalSemaphore_t* extSem_out, const cudaExternalSemaphoreHandleDesc* semHandleDesc) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaSignalExternalSemaphoresAsync(const cudaExternalSemaphore_t* extSemArray, const cudaExternalSemaphoreSignalParams* paramsArray, unsigned int numExtSems, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaWaitExternalSemaphoresAsync(const cudaExternalSemaphore_t* extSemArray, const cudaExternalSemaphoreWaitParams* paramsArray, unsigned int numExtSems, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDestroyExternalSemaphore(cudaExternalSemaphore_t extSem) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaFuncSetCacheConfig(const void* func, cudaFuncCache cacheConfig) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaFuncGetAttributes(cudaFuncAttributes* attr, const void* func) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaFuncSetAttribute(const void* func, cudaFuncAttribute attr, int value) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaLaunchHostFunc(cudaStream_t stream, cudaHostFn_t fn, void* userData) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaFuncSetSharedMemConfig(const void* func, cudaSharedMemConfig config) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, const void* func, int blockSize, size_t dynamicSMemSize) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, const void* func, int numBlocks, int blockSize) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int* numBlocks, const void* func, int blockSize, size_t dynamicSMemSize, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMallocManaged(void** devPtr, size_t size, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMalloc(void** devPtr, size_t size) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMallocHost(void** ptr, size_t size) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMallocPitch(void** devPtr, size_t* pitch, size_t width, size_t height) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMallocArray(cudaArray_t* array, const cudaChannelFormatDesc* desc, size_t width, size_t height, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaFree(void* devPtr) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaFreeHost(void* ptr) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaFreeArray(cudaArray_t array) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaFreeMipmappedArray(cudaMipmappedArray_t mipmappedArray) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaHostAlloc(void** pHost, size_t size, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaHostRegister(void* ptr, size_t size, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaHostUnregister(void* ptr) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaHostGetDevicePointer(void** pDevice, void* pHost, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaHostGetFlags(unsigned int* pFlags, void* pHost) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMalloc3D(cudaPitchedPtr* pitchedDevPtr, cudaExtent extent) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMalloc3DArray(cudaArray_t* array, const cudaChannelFormatDesc* desc, cudaExtent extent, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMallocMipmappedArray(cudaMipmappedArray_t* mipmappedArray, const cudaChannelFormatDesc* desc, cudaExtent extent, unsigned int numLevels, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetMipmappedArrayLevel(cudaArray_t* levelArray, cudaMipmappedArray_const_t mipmappedArray, unsigned int level) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemcpy3D(const cudaMemcpy3DParms* p) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemcpy3DPeer(const cudaMemcpy3DPeerParms* p) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemcpy3DAsync(const cudaMemcpy3DParms* p, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemcpy3DPeerAsync(const cudaMemcpy3DPeerParms* p, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemGetInfo(size_t* free, size_t* total) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaArrayGetInfo(cudaChannelFormatDesc* desc, cudaExtent* extent, unsigned int* flags, cudaArray_t array) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaArrayGetPlane(cudaArray_t* pPlaneArray, cudaArray_t hArray, unsigned int planeIdx) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaArrayGetMemoryRequirements(cudaArrayMemoryRequirements* memoryRequirements, cudaArray_t array, int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMipmappedArrayGetMemoryRequirements(cudaArrayMemoryRequirements* memoryRequirements, cudaMipmappedArray_t mipmap, int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaArrayGetSparseProperties(cudaArraySparseProperties* sparseProperties, cudaArray_t array) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMipmappedArrayGetSparseProperties(cudaArraySparseProperties* sparseProperties, cudaMipmappedArray_t mipmap) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemcpy(void* dst, const void* src, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemcpyPeer(void* dst, int dstDevice, const void* src, int srcDevice, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil cdef 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 cdef 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 cdef 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 cdef 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 cdef cudaError_t cudaMemcpyAsync(void* dst, const void* src, size_t count, cudaMemcpyKind kind, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemcpyPeerAsync(void* dst, int dstDevice, const void* src, int srcDevice, size_t count, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef 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 cdef 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 cdef 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 cdef cudaError_t cudaMemset(void* devPtr, int value, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemset2D(void* devPtr, size_t pitch, int value, size_t width, size_t height) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemset3D(cudaPitchedPtr pitchedDevPtr, int value, cudaExtent extent) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemsetAsync(void* devPtr, int value, size_t count, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemset2DAsync(void* devPtr, size_t pitch, int value, size_t width, size_t height, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemset3DAsync(cudaPitchedPtr pitchedDevPtr, int value, cudaExtent extent, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPrefetchAsync(const void* devPtr, size_t count, int dstDevice, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPrefetchAsync_v2(const void* devPtr, size_t count, cudaMemLocation location, unsigned int flags, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemAdvise(const void* devPtr, size_t count, cudaMemoryAdvise advice, int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemAdvise_v2(const void* devPtr, size_t count, cudaMemoryAdvise advice, cudaMemLocation location) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemRangeGetAttribute(void* data, size_t dataSize, cudaMemRangeAttribute attribute, const void* devPtr, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemRangeGetAttributes(void** data, size_t* dataSizes, cudaMemRangeAttribute* attributes, size_t numAttributes, const void* devPtr, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemcpyToArray(cudaArray_t dst, size_t wOffset, size_t hOffset, const void* src, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemcpyFromArray(void* dst, cudaArray_const_t src, size_t wOffset, size_t hOffset, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil cdef 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 cdef 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 cdef 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 cdef cudaError_t cudaMallocAsync(void** devPtr, size_t size, cudaStream_t hStream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaFreeAsync(void* devPtr, cudaStream_t hStream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolTrimTo(cudaMemPool_t memPool, size_t minBytesToKeep) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolSetAttribute(cudaMemPool_t memPool, cudaMemPoolAttr attr, void* value) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolGetAttribute(cudaMemPool_t memPool, cudaMemPoolAttr attr, void* value) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolSetAccess(cudaMemPool_t memPool, const cudaMemAccessDesc* descList, size_t count) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolGetAccess(cudaMemAccessFlags* flags, cudaMemPool_t memPool, cudaMemLocation* location) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolCreate(cudaMemPool_t* memPool, const cudaMemPoolProps* poolProps) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolDestroy(cudaMemPool_t memPool) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMallocFromPoolAsync(void** ptr, size_t size, cudaMemPool_t memPool, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolExportToShareableHandle(void* shareableHandle, cudaMemPool_t memPool, cudaMemAllocationHandleType handleType, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolImportFromShareableHandle(cudaMemPool_t* memPool, void* shareableHandle, cudaMemAllocationHandleType handleType, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolExportPointer(cudaMemPoolPtrExportData* exportData, void* ptr) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaMemPoolImportPointer(void** ptr, cudaMemPool_t memPool, cudaMemPoolPtrExportData* exportData) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaPointerGetAttributes(cudaPointerAttributes* attributes, const void* ptr) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceCanAccessPeer(int* canAccessPeer, int device, int peerDevice) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceEnablePeerAccess(int peerDevice, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceDisablePeerAccess(int peerDevice) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsUnregisterResource(cudaGraphicsResource_t resource) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsResourceSetMapFlags(cudaGraphicsResource_t resource, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsMapResources(int count, cudaGraphicsResource_t* resources, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsUnmapResources(int count, cudaGraphicsResource_t* resources, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsResourceGetMappedPointer(void** devPtr, size_t* size, cudaGraphicsResource_t resource) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsSubResourceGetMappedArray(cudaArray_t* array, cudaGraphicsResource_t resource, unsigned int arrayIndex, unsigned int mipLevel) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsResourceGetMappedMipmappedArray(cudaMipmappedArray_t* mipmappedArray, cudaGraphicsResource_t resource) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetChannelDesc(cudaChannelFormatDesc* desc, cudaArray_const_t array) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaChannelFormatDesc cudaCreateChannelDesc(int x, int y, int z, int w, cudaChannelFormatKind f) nogil cdef cudaError_t cudaCreateTextureObject(cudaTextureObject_t* pTexObject, const cudaResourceDesc* pResDesc, const cudaTextureDesc* pTexDesc, const cudaResourceViewDesc* pResViewDesc) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDestroyTextureObject(cudaTextureObject_t texObject) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetTextureObjectResourceDesc(cudaResourceDesc* pResDesc, cudaTextureObject_t texObject) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetTextureObjectTextureDesc(cudaTextureDesc* pTexDesc, cudaTextureObject_t texObject) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetTextureObjectResourceViewDesc(cudaResourceViewDesc* pResViewDesc, cudaTextureObject_t texObject) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaCreateSurfaceObject(cudaSurfaceObject_t* pSurfObject, const cudaResourceDesc* pResDesc) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDestroySurfaceObject(cudaSurfaceObject_t surfObject) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetSurfaceObjectResourceDesc(cudaResourceDesc* pResDesc, cudaSurfaceObject_t surfObject) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDriverGetVersion(int* driverVersion) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaRuntimeGetVersion(int* runtimeVersion) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphCreate(cudaGraph_t* pGraph, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddKernelNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaKernelNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphKernelNodeGetParams(cudaGraphNode_t node, cudaKernelNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphKernelNodeSetParams(cudaGraphNode_t node, const cudaKernelNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphKernelNodeCopyAttributes(cudaGraphNode_t hSrc, cudaGraphNode_t hDst) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphKernelNodeGetAttribute(cudaGraphNode_t hNode, cudaKernelNodeAttrID attr, cudaKernelNodeAttrValue* value_out) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphKernelNodeSetAttribute(cudaGraphNode_t hNode, cudaKernelNodeAttrID attr, const cudaKernelNodeAttrValue* value) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddMemcpyNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaMemcpy3DParms* pCopyParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef 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 cdef cudaError_t cudaGraphMemcpyNodeGetParams(cudaGraphNode_t node, cudaMemcpy3DParms* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphMemcpyNodeSetParams(cudaGraphNode_t node, const cudaMemcpy3DParms* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphMemcpyNodeSetParams1D(cudaGraphNode_t node, void* dst, const void* src, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddMemsetNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaMemsetParams* pMemsetParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphMemsetNodeGetParams(cudaGraphNode_t node, cudaMemsetParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphMemsetNodeSetParams(cudaGraphNode_t node, const cudaMemsetParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddHostNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaHostNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphHostNodeGetParams(cudaGraphNode_t node, cudaHostNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphHostNodeSetParams(cudaGraphNode_t node, const cudaHostNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddChildGraphNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaGraph_t childGraph) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphChildGraphNodeGetGraph(cudaGraphNode_t node, cudaGraph_t* pGraph) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddEmptyNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddEventRecordNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphEventRecordNodeGetEvent(cudaGraphNode_t node, cudaEvent_t* event_out) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphEventRecordNodeSetEvent(cudaGraphNode_t node, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddEventWaitNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphEventWaitNodeGetEvent(cudaGraphNode_t node, cudaEvent_t* event_out) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphEventWaitNodeSetEvent(cudaGraphNode_t node, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddExternalSemaphoresSignalNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaExternalSemaphoreSignalNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExternalSemaphoresSignalNodeGetParams(cudaGraphNode_t hNode, cudaExternalSemaphoreSignalNodeParams* params_out) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExternalSemaphoresSignalNodeSetParams(cudaGraphNode_t hNode, const cudaExternalSemaphoreSignalNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddExternalSemaphoresWaitNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, const cudaExternalSemaphoreWaitNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExternalSemaphoresWaitNodeGetParams(cudaGraphNode_t hNode, cudaExternalSemaphoreWaitNodeParams* params_out) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExternalSemaphoresWaitNodeSetParams(cudaGraphNode_t hNode, const cudaExternalSemaphoreWaitNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddMemAllocNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaMemAllocNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphMemAllocNodeGetParams(cudaGraphNode_t node, cudaMemAllocNodeParams* params_out) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddMemFreeNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, void* dptr) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphMemFreeNodeGetParams(cudaGraphNode_t node, void* dptr_out) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGraphMemTrim(int device) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceGetGraphMemAttribute(int device, cudaGraphMemAttributeType attr, void* value) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaDeviceSetGraphMemAttribute(int device, cudaGraphMemAttributeType attr, void* value) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphClone(cudaGraph_t* pGraphClone, cudaGraph_t originalGraph) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphNodeFindInClone(cudaGraphNode_t* pNode, cudaGraphNode_t originalNode, cudaGraph_t clonedGraph) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphNodeGetType(cudaGraphNode_t node, cudaGraphNodeType* pType) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphGetNodes(cudaGraph_t graph, cudaGraphNode_t* nodes, size_t* numNodes) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphGetRootNodes(cudaGraph_t graph, cudaGraphNode_t* pRootNodes, size_t* pNumRootNodes) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphGetEdges(cudaGraph_t graph, cudaGraphNode_t* from_, cudaGraphNode_t* to, size_t* numEdges) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphGetEdges_v2(cudaGraph_t graph, cudaGraphNode_t* from_, cudaGraphNode_t* to, cudaGraphEdgeData* edgeData, size_t* numEdges) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphNodeGetDependencies(cudaGraphNode_t node, cudaGraphNode_t* pDependencies, size_t* pNumDependencies) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphNodeGetDependencies_v2(cudaGraphNode_t node, cudaGraphNode_t* pDependencies, cudaGraphEdgeData* edgeData, size_t* pNumDependencies) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphNodeGetDependentNodes(cudaGraphNode_t node, cudaGraphNode_t* pDependentNodes, size_t* pNumDependentNodes) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphNodeGetDependentNodes_v2(cudaGraphNode_t node, cudaGraphNode_t* pDependentNodes, cudaGraphEdgeData* edgeData, size_t* pNumDependentNodes) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddDependencies(cudaGraph_t graph, const cudaGraphNode_t* from_, const cudaGraphNode_t* to, size_t numDependencies) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddDependencies_v2(cudaGraph_t graph, const cudaGraphNode_t* from_, const cudaGraphNode_t* to, const cudaGraphEdgeData* edgeData, size_t numDependencies) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphRemoveDependencies(cudaGraph_t graph, const cudaGraphNode_t* from_, const cudaGraphNode_t* to, size_t numDependencies) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphRemoveDependencies_v2(cudaGraph_t graph, const cudaGraphNode_t* from_, const cudaGraphNode_t* to, const cudaGraphEdgeData* edgeData, size_t numDependencies) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphDestroyNode(cudaGraphNode_t node) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphInstantiate(cudaGraphExec_t* pGraphExec, cudaGraph_t graph, unsigned long long flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphInstantiateWithFlags(cudaGraphExec_t* pGraphExec, cudaGraph_t graph, unsigned long long flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphInstantiateWithParams(cudaGraphExec_t* pGraphExec, cudaGraph_t graph, cudaGraphInstantiateParams* instantiateParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecGetFlags(cudaGraphExec_t graphExec, unsigned long long* flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecKernelNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaKernelNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecMemcpyNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaMemcpy3DParms* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecMemcpyNodeSetParams1D(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, void* dst, const void* src, size_t count, cudaMemcpyKind kind) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecMemsetNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaMemsetParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecHostNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, const cudaHostNodeParams* pNodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecChildGraphNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t node, cudaGraph_t childGraph) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecEventRecordNodeSetEvent(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecEventWaitNodeSetEvent(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, cudaEvent_t event) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecExternalSemaphoresSignalNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, const cudaExternalSemaphoreSignalNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecExternalSemaphoresWaitNodeSetParams(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, const cudaExternalSemaphoreWaitNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphNodeSetEnabled(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, unsigned int isEnabled) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphNodeGetEnabled(cudaGraphExec_t hGraphExec, cudaGraphNode_t hNode, unsigned int* isEnabled) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecUpdate(cudaGraphExec_t hGraphExec, cudaGraph_t hGraph, cudaGraphExecUpdateResultInfo* resultInfo) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphUpload(cudaGraphExec_t graphExec, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphLaunch(cudaGraphExec_t graphExec, cudaStream_t stream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecDestroy(cudaGraphExec_t graphExec) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphDestroy(cudaGraph_t graph) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphDebugDotPrint(cudaGraph_t graph, const char* path, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaUserObjectCreate(cudaUserObject_t* object_out, void* ptr, cudaHostFn_t destroy, unsigned int initialRefcount, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaUserObjectRetain(cudaUserObject_t object, unsigned int count) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaUserObjectRelease(cudaUserObject_t object, unsigned int count) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphRetainUserObject(cudaGraph_t graph, cudaUserObject_t object, unsigned int count, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphReleaseUserObject(cudaGraph_t graph, cudaUserObject_t object, unsigned int count) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddNode(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, size_t numDependencies, cudaGraphNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphAddNode_v2(cudaGraphNode_t* pGraphNode, cudaGraph_t graph, const cudaGraphNode_t* pDependencies, const cudaGraphEdgeData* dependencyData, size_t numDependencies, cudaGraphNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphNodeSetParams(cudaGraphNode_t node, cudaGraphNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphExecNodeSetParams(cudaGraphExec_t graphExec, cudaGraphNode_t node, cudaGraphNodeParams* nodeParams) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphConditionalHandleCreate(cudaGraphConditionalHandle* pHandle_out, cudaGraph_t graph, unsigned int defaultLaunchValue, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetDriverEntryPoint(const char* symbol, void** funcPtr, unsigned long long flags, cudaDriverEntryPointQueryResult* driverStatus) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetDriverEntryPointByVersion(const char* symbol, void** funcPtr, unsigned int cudaVersion, unsigned long long flags, cudaDriverEntryPointQueryResult* driverStatus) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetExportTable(const void** ppExportTable, const cudaUUID_t* pExportTableId) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGetKernel(cudaKernel_t* kernelPtr, const void* entryFuncAddr) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaPitchedPtr make_cudaPitchedPtr(void* d, size_t p, size_t xsz, size_t ysz) nogil cdef cudaPos make_cudaPos(size_t x, size_t y, size_t z) nogil cdef cudaExtent make_cudaExtent(size_t w, size_t h, size_t d) nogil cdef cudaError_t cudaGraphicsEGLRegisterImage(cudaGraphicsResource** pCudaResource, EGLImageKHR image, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEGLStreamConsumerConnect(cudaEglStreamConnection* conn, EGLStreamKHR eglStream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEGLStreamConsumerConnectWithFlags(cudaEglStreamConnection* conn, EGLStreamKHR eglStream, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEGLStreamConsumerDisconnect(cudaEglStreamConnection* conn) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEGLStreamConsumerAcquireFrame(cudaEglStreamConnection* conn, cudaGraphicsResource_t* pCudaResource, cudaStream_t* pStream, unsigned int timeout) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEGLStreamConsumerReleaseFrame(cudaEglStreamConnection* conn, cudaGraphicsResource_t pCudaResource, cudaStream_t* pStream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEGLStreamProducerConnect(cudaEglStreamConnection* conn, EGLStreamKHR eglStream, EGLint width, EGLint height) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEGLStreamProducerDisconnect(cudaEglStreamConnection* conn) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEGLStreamProducerPresentFrame(cudaEglStreamConnection* conn, cudaEglFrame eglframe, cudaStream_t* pStream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEGLStreamProducerReturnFrame(cudaEglStreamConnection* conn, cudaEglFrame* eglframe, cudaStream_t* pStream) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsResourceGetMappedEglFrame(cudaEglFrame* eglFrame, cudaGraphicsResource_t resource, unsigned int index, unsigned int mipLevel) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaEventCreateFromEGLSync(cudaEvent_t* phEvent, EGLSyncKHR eglSync, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaProfilerStart() except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaProfilerStop() except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGLGetDevices(unsigned int* pCudaDeviceCount, int* pCudaDevices, unsigned int cudaDeviceCount, cudaGLDeviceList deviceList) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsGLRegisterImage(cudaGraphicsResource** resource, GLuint image, GLenum target, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsGLRegisterBuffer(cudaGraphicsResource** resource, GLuint buffer, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaVDPAUGetDevice(int* device, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaVDPAUSetVDPAUDevice(int device, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsVDPAURegisterVideoSurface(cudaGraphicsResource** resource, VdpVideoSurface vdpSurface, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t cudaGraphicsVDPAURegisterOutputSurface(cudaGraphicsResource** resource, VdpOutputSurface vdpSurface, unsigned int flags) except ?cudaErrorCallRequiresNewerDriver nogil cdef cudaError_t getLocalRuntimeVersion(int* runtimeVersion) except ?cudaErrorCallRequiresNewerDriver nogil cdef enum: cudaHostAllocDefault = 0 cdef enum: cudaHostAllocPortable = 1 cdef enum: cudaHostAllocMapped = 2 cdef enum: cudaHostAllocWriteCombined = 4 cdef enum: cudaHostRegisterDefault = 0 cdef enum: cudaHostRegisterPortable = 1 cdef enum: cudaHostRegisterMapped = 2 cdef enum: cudaHostRegisterIoMemory = 4 cdef enum: cudaHostRegisterReadOnly = 8 cdef enum: cudaPeerAccessDefault = 0 cdef enum: cudaStreamDefault = 0 cdef enum: cudaStreamNonBlocking = 1 cdef enum: cudaStreamLegacy = 1 cdef enum: cudaStreamPerThread = 2 cdef enum: cudaEventDefault = 0 cdef enum: cudaEventBlockingSync = 1 cdef enum: cudaEventDisableTiming = 2 cdef enum: cudaEventInterprocess = 4 cdef enum: cudaEventRecordDefault = 0 cdef enum: cudaEventRecordExternal = 1 cdef enum: cudaEventWaitDefault = 0 cdef enum: cudaEventWaitExternal = 1 cdef enum: cudaDeviceScheduleAuto = 0 cdef enum: cudaDeviceScheduleSpin = 1 cdef enum: cudaDeviceScheduleYield = 2 cdef enum: cudaDeviceScheduleBlockingSync = 4 cdef enum: cudaDeviceBlockingSync = 4 cdef enum: cudaDeviceScheduleMask = 7 cdef enum: cudaDeviceMapHost = 8 cdef enum: cudaDeviceLmemResizeToMax = 16 cdef enum: cudaDeviceSyncMemops = 128 cdef enum: cudaDeviceMask = 255 cdef enum: cudaArrayDefault = 0 cdef enum: cudaArrayLayered = 1 cdef enum: cudaArraySurfaceLoadStore = 2 cdef enum: cudaArrayCubemap = 4 cdef enum: cudaArrayTextureGather = 8 cdef enum: cudaArrayColorAttachment = 32 cdef enum: cudaArraySparse = 64 cdef enum: cudaArrayDeferredMapping = 128 cdef enum: cudaIpcMemLazyEnablePeerAccess = 1 cdef enum: cudaMemAttachGlobal = 1 cdef enum: cudaMemAttachHost = 2 cdef enum: cudaMemAttachSingle = 4 cdef enum: cudaOccupancyDefault = 0 cdef enum: cudaOccupancyDisableCachingOverride = 1 cdef enum: cudaCpuDeviceId = -1 cdef enum: cudaInvalidDeviceId = -2 cdef enum: cudaInitDeviceFlagsAreValid = 1 cdef enum: cudaCooperativeLaunchMultiDeviceNoPreSync = 1 cdef enum: cudaCooperativeLaunchMultiDeviceNoPostSync = 2 cdef enum: cudaArraySparsePropertiesSingleMipTail = 1 cdef enum: CUDA_IPC_HANDLE_SIZE = 64 cdef enum: cudaExternalMemoryDedicated = 1 cdef enum: cudaExternalSemaphoreSignalSkipNvSciBufMemSync = 1 cdef enum: cudaExternalSemaphoreWaitSkipNvSciBufMemSync = 2 cdef enum: cudaNvSciSyncAttrSignal = 1 cdef enum: cudaNvSciSyncAttrWait = 2 cdef enum: cudaGraphKernelNodePortDefault = 0 cdef enum: cudaGraphKernelNodePortProgrammatic = 1 cdef enum: cudaGraphKernelNodePortLaunchCompletion = 2 cdef enum: cudaStreamAttributeAccessPolicyWindow = 1 cdef enum: cudaStreamAttributeSynchronizationPolicy = 3 cdef enum: cudaStreamAttributeMemSyncDomainMap = 9 cdef enum: cudaStreamAttributeMemSyncDomain = 10 cdef enum: cudaStreamAttributePriority = 8 cdef enum: cudaKernelNodeAttributeAccessPolicyWindow = 1 cdef enum: cudaKernelNodeAttributeCooperative = 2 cdef enum: cudaKernelNodeAttributePriority = 8 cdef enum: cudaKernelNodeAttributeClusterDimension = 4 cdef enum: cudaKernelNodeAttributeClusterSchedulingPolicyPreference = 5 cdef enum: cudaKernelNodeAttributeMemSyncDomainMap = 9 cdef enum: cudaKernelNodeAttributeMemSyncDomain = 10 cdef enum: cudaKernelNodeAttributePreferredSharedMemoryCarveout = 14 cdef enum: cudaKernelNodeAttributeDeviceUpdatableKernelNode = 13 cdef enum: cudaSurfaceType1D = 1 cdef enum: cudaSurfaceType2D = 2 cdef enum: cudaSurfaceType3D = 3 cdef enum: cudaSurfaceTypeCubemap = 12 cdef enum: cudaSurfaceType1DLayered = 241 cdef enum: cudaSurfaceType2DLayered = 242 cdef enum: cudaSurfaceTypeCubemapLayered = 252 cdef enum: cudaTextureType1D = 1 cdef enum: cudaTextureType2D = 2 cdef enum: cudaTextureType3D = 3 cdef enum: cudaTextureTypeCubemap = 12 cdef enum: cudaTextureType1DLayered = 241 cdef enum: cudaTextureType2DLayered = 242 cdef enum: cudaTextureTypeCubemapLayered = 252 cdef enum: CUDART_VERSION = 12060 cdef enum: __CUDART_API_VERSION = 12060 cdef enum: CUDA_EGL_MAX_PLANES = 3