Coverage for cuda / bindings / cydriver.pyx: 66.12%
983 statements
« prev ^ index » next coverage.py v7.13.5, created at 2026-03-25 01:07 +0000
« prev ^ index » next coverage.py v7.13.5, created at 2026-03-25 01:07 +0000
1# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved.
2# SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE
4# This code was automatically generated with version 13.2.0, generator version 8797618. Do not modify it directly.
5cimport cuda.bindings._bindings.cydriver as cydriver
7cdef CUresult cuGetErrorString(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil:
8 return cydriver._cuGetErrorString(error, pStr) 2BK`w
10cdef CUresult cuGetErrorName(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil:
11 return cydriver._cuGetErrorName(error, pStr) 2Cr9kDr!kBK`w[V3b9gTi
13cdef CUresult cuInit(unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
14 return cydriver._cuInit(Flags) 2a {w#k|wEr}w~waxbxcxdxexfxgxhxixjxkxlxmxnxoxpxqxFrGrHrIrJrKrLrMrNrOrPrQrRrSrTrUrVrWrXrYrZr0r1r2r3r4r5r6rrxsxtxuxvxwxxxyxzxAxBxCxDxExFxGx
16cdef CUresult cuDriverGetVersion(int* driverVersion) except ?CUDA_ERROR_NOT_FOUND nogil:
17 return cydriver._cuDriverGetVersion(driverVersion) 2a *c+cUi]V7rrcCKppqprpsptpupvpwpxpypzpApBpCpDpEpFpGpHpIpJpKpLpMpNpOpPpQpRpSpTpHxDK^VUp_VVpIxJxKxEKLxMx`V{V|V}V~VaWbWcWdWeWfWgWhWiWjWkWlWmWnWoWpWqWrWsWtWuWvWwWxWyWzWAWBWCWDWEWFWNxOx$k
19cdef CUresult cuDeviceGet(CUdevice* device, int ordinal) except ?CUDA_ERROR_NOT_FOUND nogil:
20 return cydriver._cuDeviceGet(device, ordinal) 2|w}w~waxbxcxdxexfxgxhxixjxkxlxmxnxox`wpxqxFrGrHrIrJrKrLrMrNrOrPrQrRrSrTrUrVrWrXrYrZr0r1r2r3r4r5r6rrxsxtxuxvxwxxxyxzxAxBxCxDxExFxGx
22cdef CUresult cuDeviceGetCount(int* count) except ?CUDA_ERROR_NOT_FOUND nogil:
23 return cydriver._cuDeviceGetCount(count) 2a PxFKGKHKIKJKKKLKMKNKOKPKQKRKSKTKUKVKWKXKYKZK0K1K2K3K4K5K6K7K8K9KQxRxSxTxGWUxVxWxXxYx%kVi'kZxWi(k)k0x1x2x3x4x5x6x7x8x9x!x#x$x%x'x(x)x*x+x,x-x.x/x:x;x=x?x@x[x]x^x_x`x{x|x}x~xaybycy*k+k4bXi4d5dYi,k-k.k/k,c6d!g#g$g%g:k;k=k?k5bZi7d8d0i@k[k]k^k-c9d'g(g)g_k`k{k1i|kdy2i}k~kal3ibl4icldlelfl6b5i!d#d6iglhliljl.c$d*g+g,g-gklllmlnl7b7i%d'd8iolplqlrl/c(d.g/g:g;gsltlulvl8b9i)d*d!iwlxlylzl:c+d=g?g@g[gAlBlClDl9b#i,d-d$iElFlGlHl;c.d]g^g_g`gIlJlKl%iLl'iMlNlOl(iPl)iQlRlSl*iTl+iUlVl!K#K$K%K'K(K)K*K+K,K-K.K/K:K;K=K?K@K[K]K^K_K`K{K|K}K~KaLbLcLdLeLfLgLhLiLjLkLlLmLnL8 oLpLqLrLsLtLuLvLwL/d:dWl;d=dP XlYlZleyfygyhyiyjykylymynyoypyqyrysytyuyvywyxyyyzyAyByCyDyWp,iXp6fYp/ : ; = ? @ 8rErxLHWyLzLALBLCLDLELFL9r!r#r$r%r'r(r)r*r+r,r-r.r/r:rscQ tcGL0lHLILJLKLLLMLNLEy7f=c?c@crc[cppqprpsptpupvpwpxpypzpApBpCpDpEpFpGpHpIpJpKpLpMpNpOpPpQpRpSp;rTp=r1l2l8fZp0p1p?r@r[r]r^r_r`r{r|r}r~rasbscsdsesfsgshsisjskslsmsnsospsqsrssstsusvs9f?dvbOLPLQLRL{g|gSL}g[ TL]c~g@d^c!bahUL[dbh]dVLch^ddh_dWL_cXL#behYL`dZL!f0Luc1L#f$f%f'fvc(f2Lfh{d`c$b3Lgh|d4Lhh5L}dih6L~d7Ljh8Lae9L{c!L%bkhlh)f#L*f$Lmh|c%Lwc}c-i3lnhwb'b~c4lohphxbyb2pIW'L5l(L6l7l8lC )L9l9g*L+L,L-L.L/L:L;L=L!l#l$lwsxsUpVp%l'l(l)l*l+l,l-l.l/l:l;l=l?l@l[l]l^l_l`l{l|l}l~lambmcmdmemfmgmhmimjmkmlmmmnmompmqmrmsmtmumvmwmxmymzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOmPmQmRmFySmTm.i(b3p?L@L/iGy:i;i=iHyUmVmWmXmbeceqh4pIyysYmZm?i0mzs1m@i)b5p[LJy[iKy]i^i_iLy2m3m4m5mdeeerh6pMyAs6m7mzbfege`i+f,f-fadhesh.f/fie1 jebdxcyccdthddedfdkeAb{iBbzc:fuhgdhd] ^ Cb9 ! # $ vh_ ;f=f?f@fwh8m9mAcid[f7p!m#m$m|i*b8p}i~iajbjNy%m'm(m)mle]Lmexh9pOy*m+mcjyhDb,mPyzhBsAhBhChCsdjejfjgjjdQykd]f-mDs!phjijjj` ldmdDhneoepeBcqe^fresekjEhEb.mRyFhljmjGhEsnjojpjqjndSyod_f/mFsrjsjHhIhteueveweJhxeyezeAe{ pdqdBeCeDerd`fEeFe:m+b#ptjujvjwj;m=m?mGeHeKhTy@m[m{f|f}f~f]m^m_m`m{mLh,bagbgsdtdcgxjIeJeKeLeCcMeyjNeOe-bDcEcFcud.b/b| :b;b=b|m?b$pzjAjBjCjUy}m~manbnPeQeMh%pVycnR FbGb@bGcHcIcJc% KcLcvdReSewdTeUeDj[bNhOhVeWePhdndgegfgenXexdggfnhgiggn]bEjFjGjHjhninjnYeZeQhknlnRhjg} IjGskg'plgmgng(pShThUhVhMcHsNc0eJj)pWhXhmnnnKj^b^L_LLjWyMjNjOjXyonpnqnrn1e2eYh*pYyIssntnHb3e4ePjogpgqgyd5eZhrgsg6e2 7ezdOcPcAd0hBdCdDd8eIbQjJbQctg1hEdFd~ abKb' ( ) * 2hbbugvgwgxg3hunvnRcGdyg+pwnxnynRj_b,pSjTjUjVjZyznAnBnCn9e`L!e4hJs0yDnEnFnWj`b-p{LXj1yYjZj0j2yGnHnInJn#e|L$e5hKs3yLsKnLn1jcbHdId6h%e'e(eSc)ezg*e+e2j7hLbMn4y8h3j4j9h5j6j7j8jJd5yKdAg.pMs9j!j!h#h,e-e.e$h/e:e;e=edbLdMd?e@e[eNdBg]e^eNn{b/p#j$j%j'jOnPnQn_e`e%h6yRnSnCgDgEgFgTnUnVnWnXn'h|bGgHgOdPdIg(j{e|e}e~eTcaf)jbfcf}bUcVcWcQd~bacebbcccdcYnec:p*j+j,j-j7yZn0n1n2ndfef(hNs8y3n4nS MbNbfcXcYcZc0c+ 1c2cRdffgfSdhfif5ngc.j/jJgKg:j;p)h*h+h6njfkf,h=p-h.h7nhc;j=j?j@j8n9n!nlfmf#n$n/hLgfb[jOsMg?pNgOgPg@p:h;h=h?h3cPs4cnf%n[p@h[h'n}L~L5c6cTdUdQsRs(n]jOb]paM9yof!y^j_j`j#y)n*n+n,npfqf]h^p_pIxSsTsJx$y`p-n.n/n{jic{pbMcM|j%y}j~jak'y:n;n=n?nrfsf^h|p(yUs@n[n]nbkjc}pdM)yck*ydkekfk+y^n_n`n{ntfuf_h~p,yVs|n}n~ngkkcaqeM-yhk.yikjkkk/yaobocodovfwf`hbq:yWseofogolklccqfM;ymk=ynkokpk?yhoiojokoxfyf{hdq@yXslomonoqkmceqgM[yrk]ysktkuk^yoopoqorozfAf|hfq_yYssotouovkncgqhMiMwk`yxkykzk{yvowoxoyoBfCf}hZs0s|y1szoAoBoAkochqjMkMBk}yCkDkEk~yCoDoEoFoDfEf~h2s3saz4sGoHolM5smMnMoMpMqMrMsMtMuMvMwMxMyMzMAMBMCMDMEMFMGMHMIMJMKMLMMMNMOMPM6s7sTiQMRMSMTMUMVMWMXMYMZM0M1M8s9s!s#s2M$s%s's(s3M4M5M6M7M8M9M$k!M#M$M%M'M(M)M*M+M,M-M.M/M:M;M=M?M@M[M]M^M_M`M{M|M)s*s+s,s-s.s/s:s;s=s?s@s[s]s^s_s`s{s|s}s~satbtctdtetftgthtitjtktltmtntotptqt}M~MaNrtstbNcNdNeNfNgNhNiNjNkNlNmNnNoNpNqNFfGfHfIfJfKfLfMfNfOfPfQfRfSfTfUfVfWfXfYfZf0f1frNsNtNuNvNwNxNyNzNANBNCNDNENFNGNHNINJNKNLN
25cdef CUresult cuDeviceGetName(char* name, int length, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
26 return cydriver._cuDeviceGetName(name, length, dev) 2+cIowLJW/d:dWliq;d=dP 3 FkGkHkIkJkKkLkMkYljqWpttutvtXpwt6faiQgRg2f3fbicixtytYpztErKWMNbz9y
28cdef CUresult cuDeviceGetUuid(CUuuid* uuid, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
29 return cydriver._cuDeviceGetUuid_v2(uuid, dev) 2kqXlZl#k,ilq8rxLLWMWNWOWPWcz7r@d!b[d]d^d_d#b`d{d$b|d}d~dae%b)f'bohphdzJycjyhDb,mPyzhBsAhBhChCsdjejfjgjjdQykd]f-mDs!phjij5c6cTdUd)y-y;y[y
31cdef CUresult cuDeviceGetLuid(char* luid, unsigned int* deviceNodeMask, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
32 return cydriver._cuDeviceGetLuid(luid, deviceNodeMask, dev)
34cdef CUresult cuDeviceTotalMem(size_t* numbytes, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
35 return cydriver._cuDeviceTotalMem_v2(numbytes, dev)
37cdef CUresult cuDeviceGetTexture1DLinearMaxWidth(size_t* maxWidthInElements, CUarray_format pformat, unsigned numChannels, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
38 return cydriver._cuDeviceGetTexture1DLinearMaxWidth(maxWidthInElements, pformat, numChannels, dev)
40cdef CUresult cuDeviceGetAttribute(int* pi, CUdevice_attribute attrib, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
41 return cydriver._cuDeviceGetAttribute(pi, attrib, dev) 2a N gbB M T U 4 NN5 b c d e f g h i j k l m n o p q r s t u D E F G ezfzdiCrAtgzBt%kVi'kWi(k)kNk7c8c9cVdO QWRWhbibjbPbkbV W X 6 QbRbSbpcSWmqnqoqOkPkQk4fRk*k+k4bXi4d5dYi,c6d!g#g$g%g=k?k5bZi7d8d0i-c9d'gSk(g)g{k1i|k2i}k~kal3ibl4icldlelfl6b5i!d#d6i.c$d*g+g,g-gmlnl7b7i%d'd8i/c(d.g/g:g;gulvl8b9i)d*d!i:c+d=g?g@g[gClDl9b#i,d-d$i;c.d]g^g_g`gKl%iLl'iMlNlOl(iPl)iQlRlSl*iTl+iUlVlTWSgpq+cUWIoVWONPNQNRNSNTNlbmbnbobTbWdXdqq8 H , - UbVbI kqrqP Xl3 sqZltq#kuq,ilqvq8rErJohzizTgUgjzkzlzmz9r!rnzozpzqzrzsz#rtzuzvzwzxzyzzzAz$rBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z4z5z6z7z8z9z!z#z$z%z'z(z)z*z+z,z-z%r.z'r/z:z;z=z?z@z(r[z]z^z_z`z{z|z}z~zaAbAcAdAeAfAgAhAiA)rjAkA*rlAmAnAoApAqArAsAtAuAvAwA+rxAyAzAAABACADAEAFAGAHAIA,r-rJAKALAMA.rNAOAPAQARASATAUA/rVA:rQ qcpbYdZdeifigi5fhiii0d=c?c@crc[cppqprpsptpupvpwpxpypzpApBpCpDpEpFpGpHpIpJpKpLpMpNpOpPpQpRpSp;rTpWA=r8fjiki?dvbCtTkDt{g|g}gEt[ li]cUk~g@d^c!bah[dbh]dch^ddh_d_c#beh`d!fXAucYA#fZA$f0A%f1A'f2Avc3A(f4Afh{d`c$bgh|dhh}dih~djhae{c%bkh)f*fmh|cwc}cUNVkwb'b~c4lohphVNxb!c3byb2pHx5lwq6l7l8lC 9l9gxqyqzqAqBqCqDqEqFq!l#l$lwsxsUpVp5A%l6A'l7A(l8A)l9A*l!A+lFt,lGt-lHt.lIt/lJt:lKt;lLt=lMt?lNt@lOt[lPt]lQt^lRt_lSt`lTt{lUt|lVt}lWt~lambm#Acm$Adm%Aem'Afm(Agm)Ahm*Aim+Ajm,Akm-Alm.Amm/Anm:Aom;Apm=Aqm?Arm@Asm[Atm]Aum^Avm_AwmxmymzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOmdzFyTm.i(b/i=iXmbeceqh4p?i0m1m@i)b[i_i5mdeeerh6pzbfege`i+f,f-fadhesh.f/fie1 jebdxcyccdthddedfdkeAb{iBbzc:fuhgdhd] ^ Cb9 ! # $ vh_ ;f@fAcid[f$m|i*b}ibj)mlemexh9pcjyhDbzhChgjjdkd]f-mjj` ldmdDhneoepeBcqe^fresekjEhEbFhGhqjndod_f/m{ pdqdBeCeDerd`fEeFe:m+btjwjGeHeKhLh,bagbgsdtdcgxjIeJeKeLeCcMeyjNeOe-bDcEcFcud.b/b| :b;b=b|m?bzjCjbnPeQeMh%pR FbGb@bGcHcIcJc% KcLcvdReSewdTeUeDj[bNhOhVeWePhdndgegfgenXexdggfnhgiggn]bEjHjYeZeQhRhjg} kgngVhMcNc0eJjnnKj^bLjOjrn1e2eYh*pHb3e4ePjogpgqgyd5eZhrgsg6e2 7ezdOcPcAd0hBdCdDd8eIbQjJbQctg1hEdFd~ abKb' ( ) * 2hbbugxgRcGdygynRj_bSjVjCn9e!e4hJsFnWj`bXj0jJn#e$e5hKs1jcbHdId6h%e'e(eSc)ezg*e+e2j7hLb8h9h8jJdKdAg.pdbLdMd?e@e[eNdBg]e^eNn{b#j'j_e`e%h'h|bGgHgOdPdIg(j{e|e}e~eTcaf)jbfcf}bUcVcWcQd~bacebbcccdcYnec*j-j2ndfef(hNsS MbNbfcXcYcZc0c+ 1c2cRdffgfSdhfif5ngc.j/jJgKg:j;p)h*h+h6njfkf,h=p-h.h7nhc;j@jlfmfWk/hLgfbMgPg?h3c4cnf%n5c6cTdUdQsRs(n]jObof`j,npfqf]h^p_pSsTs/n{jic|jak?nrfsf^h|p]nbkjcckfk{ntfuf_h~p~ngkkchkkkdovfwf`hbqgolklcmkpkkoxfyf{hdqnoqkmcrkukrozfAf|hfquovkncwkzkyoBfCf}hZs0sBoAkocBkEkFoDfEf~h2s3sKx5sLxMxNx6s7sTi8s9s!s#sOx$s%s's(s$k)s*s+s,s-s.s/s:s;s=s?s@s[s]s^s_s`s{s|s}s~satbtctdtetftgthtitjtktltmtntotptqt`ArtstFfGfHfIfJfKfLfMfNfOfPfQfRfSfTfUfVfWfXfYfZf0f1fKo
43cdef CUresult cuDeviceGetHostAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
44 return cydriver._cuDeviceGetHostAtomicCapabilities(capabilities, operations, count, dev)
46cdef CUresult cuDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, CUdevice dev, int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
47 return cydriver._cuDeviceGetNvSciSyncAttributes(nvSciSyncAttrList, dev, flags)
49cdef CUresult cuDeviceSetMemPool(CUdevice dev, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
50 return cydriver._cuDeviceSetMemPool(dev, pool) 2WN
52cdef CUresult cuDeviceGetMemPool(CUmemoryPool* pool, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
53 return cydriver._cuDeviceGetMemPool(pool, dev) 2WbXbYbv 7 w x y 5 z A TgUg8fjiki?dliC .i?i@iie1 jebdxcyccdthddedfdkeAb{iBbzc:fuhgdhd|iyhEhjgKj6e2 7ezdOcPcAd0hBdCdDd8eIbQjJbQctg1hEdFdRjWj7hLg]j{jbkgklkqkvkAkFfGfHfIfJfKfLfMfNfOfPfQfRfSfTfUfVfWfXfYfZf0f1fKo
55cdef CUresult cuDeviceGetDefaultMemPool(CUmemoryPool* pool_out, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
56 return cydriver._cuDeviceGetDefaultMemPool(pool_out, dev) 2WN
58cdef CUresult cuDeviceGetExecAffinitySupport(int* pi, CUexecAffinityType typename, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
59 return cydriver._cuDeviceGetExecAffinitySupport(pi, typename, dev)
61cdef CUresult cuFlushGPUDirectRDMAWrites(CUflushGPUDirectRDMAWritesTarget target, CUflushGPUDirectRDMAWritesScope scope) except ?CUDA_ERROR_NOT_FOUND nogil:
62 return cydriver._cuFlushGPUDirectRDMAWrites(target, scope)
64cdef CUresult cuDeviceGetProperties(CUdevprop* prop, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
65 return cydriver._cuDeviceGetProperties(prop, dev)
67cdef CUresult cuDeviceComputeCapability(int* major, int* minor, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
68 return cydriver._cuDeviceComputeCapability(major, minor, dev)
70cdef CUresult cuDevicePrimaryCtxRetain(CUcontext* pctx, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
71 return cydriver._cuDevicePrimaryCtxRetain(pctx, dev) 2{wFrGrHrIrJrKrLrMrNrOrPrQrRrSrTrUrVrWrXrYrZr0r1r2r3r4r5r6r
73cdef CUresult cuDevicePrimaryCtxRelease(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
74 return cydriver._cuDevicePrimaryCtxRelease_v2(dev) 2WWXWYWZW0W1W2W3W4W5W6W7W8W9W!W#W$W%W'W(W)W*W+W,W-W.W/W:W
76cdef CUresult cuDevicePrimaryCtxSetFlags(CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
77 return cydriver._cuDevicePrimaryCtxSetFlags_v2(dev, flags)
79cdef CUresult cuDevicePrimaryCtxGetState(CUdevice dev, unsigned int* flags, int* active) except ?CUDA_ERROR_NOT_FOUND nogil:
80 return cydriver._cuDevicePrimaryCtxGetState(dev, flags, active)
82cdef CUresult cuDevicePrimaryCtxReset(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
83 return cydriver._cuDevicePrimaryCtxReset_v2(dev)
85cdef CUresult cuCtxCreate(CUcontext* pctx, CUctxCreateParams* ctxCreateParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
86 return cydriver._cuCtxCreate_v4(pctx, ctxCreateParams, flags, dev) 2|w}w~waxbxcxdxexfxgxhxixjxkxlxmxnxoxpxqxrxsxtxuxvxwxxxyxzxAxBxCxDxExFxGx
88cdef CUresult cuCtxDestroy(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
89 return cydriver._cuCtxDestroy_v2(ctx) 2;W=W?W@W[W]W^W_W`W{W|W}W~WaXbXcXdXeXfXgXhXiXjXkXlXmXnXoXpXqXrXsXtXuXvXwXxX
91cdef CUresult cuCtxPushCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
92 return cydriver._cuCtxPushCurrent_v2(ctx) 2mi
94cdef CUresult cuCtxPopCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
95 return cydriver._cuCtxPopCurrent_v2(pctx) 2XNYNZN0N1N2N3N4N5N6N7N8N9N!N#N$N%N'N(N)N*N+N,N-N.N/N:N;N=N?N@N[N]N{A|A}A~AaBbBcBdBeBfBgBhBiBjBkBlBmBnBoBpBqBrBsBtBuBvBXtwBxB^N_NyBzBABBBCBDBEBFBGBHBIBJBKB`NLBMBNBOBPBQBRBSBTBUBVBWBXBYB{NYtZtZB0B|N1B2B3B4B5B6B7B8B9B!B#B$B%B}N0t1t'B(B~NaObO)B*B+B,B-B.BcOdO/B:B;B=B?B@B[B]B^B_B`B{B|B}B~BaCbC2t3tcCdCeCfCgChCiCjCkClCmCnCoCpCqCrCsC4t5ttCuCvCwCxCyCzCACBCCCDCECFCGCHCICJC6t7tKCLCMCNCOCPCQCRCSCTCUCVCWCXCYCZC0C8t9t1C2C3C4C5C6C7C8C9C!C#C$C%C'C(C)C*C+C,C-C.C/C:C;C=C?C@C[C]C^C_CeOfOgOhOiOjOkOlOmOnOoOpOqOrOsOtOuOvOwOxOyOzOAOBOCODOEOFOGOHOIOJOKOLOMONOOOPOQOROSOTOUOVOWOXOYOZO0O1O2O3O4O5O6O7O8O9O!O#O$O%O'O(O)O*O+O,O-O.O/O:O;O=O?O@O[O]O^O_O`O{O|O}O~OaPbPcPdPePfPgPhPiPjPkPlPmPnPoPpPqPrPsPtPuPvPwPxPyPzPAPBPCPDPEPFPGPHPIPJPKPLPMPNPOPPPQPRPSPTPUPVPWPXPYPZP0P1P2P3P4P5P6P7P8P9P!P#P$P%P'P(P)P*P+P,P-P.P/P:P;P=P?P@P[P]P^P_P`P{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQqQrQsQtQuQvQwQxQyQzQAQBQCQDQEQFQGQHQIQJQKQLQMQNQOQPQQQRQSQTQUQVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Q,Q-Q.Q/Q:Q;Q=Q?Q@Q[Q]Q^Q_Q`Q{Q|Q}Q~QaRbRcRdReRfRgRhRiRjRkRlRmRnRoRpRqRrRsRtRuRvRwRxRyRzRAR`C{C|C}CBRCR~CaD!t#tbDcDdDeDfDDRgDhDiDERjDkDlDmDnDFRoDpDqDrDsDGRHRtDuD$t%tvDwDxDyDzDIRADBDCDJRDDEDFDGDHD't(tIDJDKDLDMDNDODPDQD)t*t+t,tGqHq-t.t/t:t;tRD=tSD?t@tTD[t]t^t_t`tUDVDWDXDYDZD0D1D{t|t2D3D4D5D6D7D8D9D!D#D$D%D'D(D)D}t~t*D+D,D-D.DKR/DLR:D;DMR=D?D@D[D]D^D_DNR`D{Daubu|D}D~DaEbEORcEPRdEeEQRfEgEhEiEjEkEcudulEmEnEoEpEqErEsEtEeufuguhuuEiujukulumunuoupuvEquwErusuxEtuuuvuwuxuyuzuAuBuCuDuEuFuGuyEHuIuzEAEBECEDEEEFEGEHEIEJEJuKuKELEMENEOEPEQERESETEUEVEWEXEYEZE0E1E2E3E4E5E6ELuMu7E8E9E!E#E$E%E'E(E)E*E+ENuOu,E-E.E/E:E;E=E?E@E[E]E^EPuQu_E`E{E|E}ERR~EaFbFSRcFdFeFfFRuSugFhFiFjFkFlFTuUumFnFoFpFqFrFsFtFuFvFVuWuwFxFyFzFAFTRBFCFDFEFFFGFHFIFJFXuYuKFLFMFNFOFPFQFRFSFZu0u1u2uTF3u4uIqJq5u6u7u8u9uUF!uVF#u$uWF%u'u(uXFYFZF0F1FURVR2F3F)u*u4F5F6F7F8FWR9F!F#FXR$F%F'F(F)F+u,u*F+F,F-F.F/F:F;F=F-u.u/u:uKqLq;u=u?u@u[u?F]u@F^u_u[F`u{u|u}u~u]F^F_F`F{F|F}F~FavbvaGbGcGdGeGfGgGhGiGjGkGlGmGnGoGcvdvpGqGrGsGtGYRuGZRvGwG0RxGyGzGAGBGCGDG1REGFGevfvGGHGIGJGKG2RLG3RMGNG4ROGPGQGRGSGTGgvhvUGVGWGXGYGZG0G1G2Givjvkvlv3Gmvnvovpvqvrvsvtv4Guv5Gvvwv6GxvyvzvAvBvCvDvEvFvGvHvIvJvKv7GLvMv8G9G!G#G$G%G'G(G)G*G+GNvOv,G-G.G/G:G;G=G?G@G[G]G^G_G`G{G|G}G~GaHbHcHdHeHPvQvfHgHhHiHjHkHlHmHnHoHpHqHRvSvrHsHtHuHvHwHxHyHzHAHBHCHTvUvDHEHFHGHHH5RIHJHKH6RLHMHNHOHVvWvPHQHRHSHTHUHXvYvVHWHXHYHZH0H1H2H3H4HZv0v5H6H7H8H9H7R!H#H$H%H'H(H)H*H+H1v2v,H-H.H/H:H;H=H?H@H3v4v5v6v[H7v8vMqNq9v!v#v$v%v]H'v^H(v)v_H*v+v,v`H8R9R!R#R{H|H}H~H$R%RaIbI-v.vcIdIeIfIgI'RhIiIjI(R)R*R+R,R-RkIlImInIoIpIqIrI.R/RsItI/v:vuIvIwIxIyI:RzIAIBI;RCIDIEIFIGIHIIIJI=R?RKILI;v=vMINIOIPIQI@RRISITI[RUIVIWIXIYIZI0I1I]R^R2I3I?v@v4I5I6I7I8I_R9I!I#I`R$I%I'I(I)I*I+I,I{R|R-I.I[v]v/I:I;I=I?I}R@I[I]I~R^I_I`I{I|I}I~IaJaSbSbJcJ^v_vdJeJfJgJhJcSiJjJkJdSlJmJnJoJpJqJrJsJeSfStJuJ`v{vvJwJxJyJzJgSAJBJCJhSiSDJEJFJGJHJIJJJKJjSkSLJMJ|v}vNJOJPJQJRJlSSJTJUJmSnSVJWJXJYJoSpSqSrSsStSuSvSwSxSySzSASBSCSDSESFSGSHSISJSKSLSMSNSOSPSQSRSSSTSUSVSWSXSYSZS0S1S2S3S4S5S6S7S8S9S!S#S$S%S'S(S)S*S+S,S-S.S/S:S;S=S?S@S[S]S^S_S`S{S|S}Smi~SaTbTcTdTeTfTgThTiTjTkTlTmTnToTpTqTrTsTtTuTvTwTxTyTzTATBTCTDTETFTGTHTITJTKTLTMTNTOTPTQTRTSTTTUTVTWTXTYTZT0T1T2T3T4T5T6T7T8T9T!T#T$T%T'T(T)T*T+T,T-T.T/T:T;T=T?T@T[T]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEU
97cdef CUresult cuCtxSetCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
98 return cydriver._cuCtxSetCurrent(ctx) 2FKGKyXzXHKIKJKKKLKAXBXCXDXEXNNFXGXHXIXJXKXLXMXNXOXPXQXRXSXTXUXVXMKNKOKPKQKRKSKTKUKVKWKXKYKZK0K1K2K3K4K5K6K7K8K9KQxRxSxTxUxVxWxXxYx%kVi'kZxWi(k)k0x1x2x3x4x5x6x7x8x9x!x#x$x%x'x(x)x*x+x,x-x.x/x:x;x=x?x@x[x]x^x_x`x{x|x}x~xaybycy*k+k4bXi4d5dYi,k-k.k/k,c6d!g#g$g%g:k;k=k?k5bZi7d8d0i@k[k]k^k-c9d'gSk(g)g_k`k{k1i|kdy2i}k~kal3ibl4icldlelfl6b5i!d#d6iglhliljl.c$d*g+g,g-gklllmlnl7b7i%d'd8iolplqlrl/c(d.g/g:g;gsltlulvl8b9i)d*d!iwlxlylzl:c+d=g?g@g[gAlBlClDl9b#i,d-d$iElFlGlHl;c.d]g^g_g`gIlJlKl%iLl'iMlNlOl(iPl)iQlRlSl*iTl+iUlVl!K#K{w$K%K'K(K)K*K+K,K-K.K/K:K;K=K?K@K[K]K^K_K`K{K|K}K~KaLbLcLdLeLfLgLhLiLjLkLlLmLnLWXoLpLqLrLsLtLXXuLvLZJ~vkqrq0Jaw1JbwXlsqYXZX0X1X2X3X4X5X6X7X8XYlZljqtq2Jcw3J4J5J#k6J7J8J9J!J#J$J%Jdwewfwgwhwiwjwkwuqlwmwnw'J,i(Jow)Jpw*JqwQg+JRgrw9X!X,Jswlqvq-Jtw#X$X%X'X(X8ryLzLALBL)XCLDLFrGrHrIrJrKrLrMrNrOrPrQrRrSrTrUrVrWrXrYrZr0r1r2r3r4r5r6rTgUg*XEL+X,X-X.X/XFL:X;XMN.J=X?XscQ tcGL0lHL@XILJL[X]X^XKLLLML_XNLVgLoWgXgMoYgZg0gni1g2g3gXkpboipi0d`X{X|X}Xqirisitiui=cviwixiyi?cziAi@cBiCiDircEiFiGiHi[cIiJiKiLiMippqprpsptpupvpwpxpypzpApBpCpDpEpFpGpHpIpJpKpLpMpNpOpPpQpRpSp;rTpWA=rYk1d2duwFU1l2lvw8fjiZpwwxw0p1pywGUHUIU?rJUKU@r[rLUMU]r^rNUOUPU_rQU`rRUSUTUUU{rVU|r}rWUXUYUZU0U1U2U3U~rasbs4U5U6Ucs7Udsesfsgshs8Uis9U!Ujs#U$U%Uks'U(U)U*U+U,U-U.Uls/U:U;U=U?U@U[Umsns]U^U_U`Uos{U|U}U~UpsqsaVbVrssstscVusdVeVfVvsgVhViV9fki?dvbOL~XCtPLTkQLDtRL{gaY|gSL}gbYEtcY[ dYliTL]ceYUkfY~ggY@dhY^ciY!bjYahUL[dkYbhlY]dVLchmY^dnYdhoY_dWL_cXL#bpYehYL`dZL!f0LqYucrY1L#fsYtY$fuYvY%fwYxY'fyYzYvcAYBY(fCY2LfhDY{dEY`cFY$b3LghGY|d4Lhh5L}dHYih6L~d7Ljh8Lae9L{c!L%bIYkhJYlhKY)f#L*f$LmhLY|c%LwcMY}cNYUN3lNonhVkOYwbPY'b~cQYRYSYTYxb!c3byb2p'LUY5l(L6l7l8l)L9l*L+L,L-L.L/L:L;LDK=L!l#l$lwsxsUpVp%l'l(l)l*l+l,l-l.l/l:l;l=l?l@l[l]l^l_l`l{l|l}l~lambmcmdmemfmgmhmimjmkmlmmmnmompmqmrmsmtmumvmwmxmymzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOmPmdzQmVYRmWYNiFySmXYTm.i(b3p?L@L/iGy:i;i=iHyUmVmWmXmbeceqh4pIyysYmZm?i0mzs1m@i)b5p[LJy[iKy]i^i_iLy2m3m4m5mdeeerh6pMyAs6m7mzbfege`i+f,f-fadhesh.f/fie1 jebdxcyccdthddedfdkeAb{iBbzc:fuhgdhd] ^ Cb9 ! # $ vh_ ;f=f?f@fwh8m9mAcid[f7p!m#m$m|i*b8p}i~iajbjNy%m'm(m)mle]Lmexh9pOy*m+mcjyhDb,mPyzhBsAhBhChCsdjejfjgjjdQykd]f-mDs!phjijjj` ldmdDhneoepeBcqe^fresekjEhEb.mRyFhljmjGhEsnjojpjqjndSyod_f/mFsrjsjHhIhteueveweJhxeyezeAe{ pdqdBeCeDerd`fEeFe:m+b#ptjujvjwj;m=m?mGeHeKhTy@m[m{f|f}f~f]m^m_m`m{mLh,bagbgsdtdcgxjIeJeKeLeCcMeyjNeOe-bDcEcFcud.b/b| :b;b=b|m?b$pzjAjBjCjUy}m~manbnPeQeMh%pVyOqcnR FbGb@bGcHcIcJc% KcLcvdReSewdTeUeDj[bNhOhVeWePhdndgegfgenXexdggfnhgiggn]bEjFjGjHjhninjnYeZeQhknlnRhjg} IjGskg'plgmgng(pShThUhVhMcHsNc0eJj)pWhXhmnnnKj^bzw^L_LLjWyMjNjOjXyonpnqnrn1e2eYh*pYyIssntnHb3e4ePjogpgqgyd5eZhrgsg6e2 7ezdOcPcAd0hBdCdDd8eIbQjJbQctg1hEdFd~ abKb' ( ) * 2hbbugvgwgxg3hunvnRcGdyg+pwnxnynRj_b,pSjTjUjVjZyznAnBnCn9e`L!e4hJs0yDnEnFnWj`b-p{LXj1yYjZj0j2yGnHnInJn#e|L$e5hKs3yLsKnLn1jcbHdId6h%e'e(eSc)ezg*e+e2j7hLbMn4y8h3j4j9h/J5j6j7j8jJd5yKdAg.pMs9j!j!h#h4g,e-e.e$h/e:e;e=edbLdMd?e@e[eNdBg]e^eNn{b/p#j$j%j'jOnPnQn_e`e%h6yRnSnCgDgEgFgTnUnVnWnXn'h|bGgHgOdPdIg(j{e|e}e~eTcaf)jbfcf}bUcVcWcQd~bacebbcccdcYnec:p*j+j,j-j7yZn0n1n2ndfef(hNs8y3n4nS MbNbfcXcYcZc0c+ 1c2cRdffgfSdhfif5ngc.j/jJgKg:j;p)h*h+h6njfkf,h=p-h.h7nhc;j=j?j@j8n9n!nlfmfWk#n$n/hLgfb[jOsMg?pNgOgPg@p:h;h=h?h3cPs4cnf%n[p@h[h'n}L~L5c6cTdUdQsRs(n]jOb]paM9yof!y^j_j`j#y)n*n+n,npfqf]h^p_pIxSsTsJx$y`p-n.n/n{jic{pbMcM|j%y}j~jak'y:n;n=n?nrfsf^h|p(yUs@n[n]nbkjc}pdM)yck*ydkekfk+y^n_n`n{ntfuf_h~p,yVs|n}n~ngkkcaqeM-yhk.yikjkkk/yaobocodovfwf`hbq:yWseofogolklccqfM;ymk=ynkokpk?yhoiojokoxfyf{hdq@yXslomonoqkmceqgM[yrk]ysktkuk^yoopoqorozfAf|hfq_yYssotouovkncgqhMiMwk`yxkykzk{yvowoxoyoBfCf}hZs0s|y1szoAoBoAkochqjMkMBk}yCkDkEk~yCoDoEoFoDfEf~h2s3saz4sGoHolMYYZYmMnM0Y1Y2YoMpMqMrM3YsMtMuMvMwMxMyMzMAMBMCM4YDMEMFMGMHM5YIM6YJMKM7YLMMMNM8YOMPMQMRMSMTMUMVMWMXM9Y!YYMZM0M1M2M3M4M5M6M7M8M9M$k!MjV#M$M%M'M(M)M*M+M,M-M.M/M:M;M=M?M@M[M]M^MPq_M`M{M|M#Y)s*s+s,s-s.s/s:s;s=s?s@s[s]s^s_s`s{s|s}s~satbtctdtetftgthtitjtktltmtntotptqt}M~MaN`ArtstbNcNdN$Y%YeNfNgNhNiNjN'Y(YkNlN)Y*YmN+Y,YnNoNpNqN-YFfQqGfHfIfJfRqKfSqLfTqUqMfVqNfOfWqPfQfRfSfTfXqYqZq0qUfVfWfXf1q2q3qYfZf4q5q0f1f.YrNsN/YtNuN:Y;Y=YvNwNxNyN?Y@Y[YzNAN]YBNCNDNENFN^Y_YGNHN`YINJN{YKNLN|Y
100cdef CUresult cuCtxGetCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
101 return cydriver._cuCtxGetCurrent(pctx) 2a }YkV~YaZbZcZdZlVeZfZgZhZPxiZjZkZXNYNZN0N1N2N3N4N5N6N7N8N9N!N#N$N%N'N(N)N*N+N,N-N.N/N:N;N=N?N@N[N]N{A|A}A~AaB6qbBcBdBeBfBgBhBiBjBkBlBmBnBoBpBqBrBsBtBuBvBXtwBxB^N_NyBzBABBBCBV DBW EBX FB6 GBQbHBRbIBSbJBpcKB`NLBMBNBOBPBQBRBSBTBUBVBWBXBYB{NYtZtZB0B|N.k1B/k2B3B6d4B!g5B#g6B$g7B%g8B:k9B;k!B#B$B%B}N0t1t'B(B~N]kaO^kbO)B9d*B'g+BSk,B(g-B)g.B_kcO`kdO/B:B;B=B?B@B[B]B^B_B`B{B|B}B~BaCbC2t3tcCdCeCilfCjlgChC$diC*gjC+gkC,glC-gmCklnClloCpCqCrCsC4t5ttCuCvCqlwCrlxCyC(dzC.gAC/gBC:gCC;gDCslECtlFCGCHCICJC6t7tKCLCMCylNCzlOCPC+dQC=gRC?gSC@gTC[gUCAlVCBlWCXCYCZC0C8t9t1C2C3CGl4CHl5C6C.d7C]g8C^g9C_g!C`g#CIl$CJl%C'C(C)C*C+C,C-C.C/C:C;C=C?C@C[C]C^C_C9keOfOgOhOiOAwjOkOlOmOnOoOpOqOrO!ksOtOuOvOwOxOyOzOAOOoBOPoCOQoDORoEOlbFOmbGOnbHOobIOJOKOLOMONOOOPOQOROSOTOUOVOWOXOYOZOUi0O1O2O3O4O5O6O7O8O9O!OhzizTg#OUg$O%O'O(O)O*O+O,O-O.O/OmVjzkzlzmz9r!rnzozpzqzrzsz#rtzuzvzwzxzyzzzAz$rBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z4z5z6z7z8z9z!z#z$z%z'z(z)z*z+z,z-z%r.z'r/z:z;z=z?z@z(r[z]z^z_z`z{z|z}z~zaAbAcAdAeAfAgAhAiA)rjAkA*rlAmAnAoApAqArAsAtAuAvAwA+rxAyAzAAABACADAEAFAGAHAIA,r-rJAKALAMA.rNAOAPAQARASATAUA/rVA:r:O.J;O=O?ObznVczlZ7rscQ tc@O0l[O]O^O_O`O{O|O}O~OaPbPcPEydPePfPgP=c?c@crc[chPiPjPkPlPmPnPoPpPqPrPsPtPuPvPwPxPyPzPAPBPCPDPEPFPGPHPIPJPKPLPMPNPOP1l2l?r@r[r]r^r_r`r{r|r}r~rasbscsdsesfsgshsisjskslsmsnsospsqsrssstsusvs9f?dPPQPRPSPTPUPVPWPXPYPZP0P1P2P3P4P5P6P7P8P9P!P#P$P%P'P(P)P*P+P,P-P.P/P:P;P=P?P@P[P]P^P_P`P{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQqQrQsQ3lnhtQuQ~cvQwQxQyQxbyb2pzQAQBQCQDQEQFQGQHQ9gIQJQKQLQMQNQOQPQQQRQSQTQUQVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Q,Q-Q.Q/Q:Q;Q=Q?Q@Q[Q]Q^Q_Q`Q{Q|Q}Q~QaRbRcRdReRfRgRhRiRjRkRlRmRnRoRpRqRrRsRtRuRvRwRxRyRzRAR`C{C|C3p}CBRCR~CaD!t#tbDcDdDVmeDWmfDDRgDcehDqhiDERjDkDYmlDZmmDnDFRoDpDqDrD5psDGRHRtDuD$t%tvDwDxD3myD4mzDIRADeeBDrhCDJRDDED6mFD7mGDHD't(tIDJD,fKD-fLDMDheNDshOD.fPD/fQD)t*tje+t,tGqHq-t.t/ted:tfd;tRD=tSDBb?tzc@tTD[tgd]thd^t_t`tUD9 VD! WD# XD$ YDvhZD_ 0D;f1D=f{t?f|t@f2Dwh3D8m4D9m5DAc6Did7D[f8D7p9D!m!D#m#D$D%D'D8p(D)D}t~t*D+D,D'm-D(m.DKR/DLRme:Dxh;DMR=D*m?D+m@D[D]D^D,m_DNR`D{Daubu|D}D~DejaEfjbEORcEPRkddE]feEQRfEgEhjhEijiEjEkEcudulEmEoenEpeoEpEqeqE^frEresEsetEeufugu.mhuuEiujukulumunuojoupjpuvEquwEodru_fsuxEturjuusjvuwuxuteyuuezuveAuweBuCuxeDuyeEuzeFuAeGuyEHuIuzECeAEDeBErdCE`fDEEeEEFeFEGEHE#pIEJEJuKuKELE=mME?mNEOEHePEKhQERE@mSE[mTE{fUE|fVE}fWE~fXE]mYE^mZE_m0E`m1E{m2E3E4Eag5E6ELuMu7E8E9EJe!EKe#E$ECc%EMe'E(ENe)EOe*E+ENuOu,E-E.b.E/b/E| :E:b;E;b=E=b?E@E[E$p]E^EPuQu_E`E{E~m|Ean}ERR~EQeaFMhbFSRcFOqdFcneFR fFFbRuGbSu@bgFGchFHciFIcjFJckF% lFKcTuLcUuvdmFRenFSeoFwdpFTeqFUerFsFtFNhuFvFVuWuwFxFyFegzFfgAFTRBFxdCFggDFEFhgFFigGFHFIFJFXuYuKFLFinMFjnNFOFZePFQhQFknRFlnSFZu0u1uIj2uTF3u4uIqJq5u6u7uTh8uUh9uUF!uVFNc#u0e$uWF%uWh'uXh(umnXFYFZF0Fzw1FURVR2F3F)u*u4F5F6Fpn7Fqn8FWR9F2e!FYh#FXR$F%Fsn'Ftn(F)F+u,u*F+Fpg,Fqg-F.F5e/FZh:Frg;Fsg=F-u.u7e/u:uKqLq;u=u?uCd@uDd[u?F]u@FJb^uQc_u[F`uEd{uFd|u}u~u]F' ^F( _F) `F* {F2h|Fbb}Fug~FvgavwgbvxgaG3hbGuncGvndGRceGGdfGyggG+phGwniGxnjGkGlGmG,pnGoGcvdvpGqGrGAnsGBntGYRuGZR!evG4hwG0RxGDnyGEnzGAGBGCG-pDG1REGFGevfvGGHGIGHnJGInKG2RLG3R$eMG5hNG4ROGPGKnQGLnRGSGTGgvhvUGVG'eWG(eXGYG)eZGzg0G*e1G+e2GivjvkvMnlv3Gmvnvovpvqvrv6jsv7jtv4Guv5GKdvvAgwv6Gxv9jyv!jzvAvBv4gCv,eDv-eEv.eFvGv/eHv:eIv;eJv=eKv7GLvMv8G@e9G[e!GNd#GBg$G]e%G^e'G(G)G/p*G+GNvOv,G-GPn.GQn/G:G`e;G%h=G?GRn@GSn[GCg]GDg^GEg_GFg`GTn{GUn|GVn}GWn~GXnaHbHcHGgdHeHPvQvfHgHhH|eiH}ejHkHTclHafmHnHbfoHcfpHqHRvSvrHsH~btHacuHebvHbcwHccxHdcyHzHAH:pBHCHTvUvDHEHFH0nGH1nHH5RIHefJH(hKH6RLH3nMH4nNHS OHMbVvNbWvfcPHXcQHYcRHZcSH0cTH+ UH1cXv2cYvRdVHffWHgfXHSdYHhfZHif0H1H2H.j3H4HZv0v5H6H7H*h8H+h9H7R!Hkf#H,h$H%H-h'H.h(H)H*H+H1v2v,H-H9n.H!n/H:Hmf;HWk=H#n?H$n@H3v4v5v[j6v[H7v8vMqNq9v!v#v;h$v=h%v]H'v^H4c(vnf)v_H*v@h+v[h,v'n`H8R9R!R#R{H|H}H]p~H$R%RaIbI-v.vcIdIeI*nfI+ngI'RhIqfiI]hjI(R)R*R+R,R-RkIlI-nmI.nnIoIpIqI{prI.R/RsItI/v:vuIvIwI;nxI=nyI:RzIsfAI^hBI;RCIDI@nEI[nFIGIHIII}pJI=R?RKILI;v=vMINIOI_nPI`nQI@RRIufSI_hTI[RUIVI|nWI}nXIYIZI0Iaq1I]R^R2I3I?v@v4I5I6Ibo7Ico8I_R9Iwf!I`h#I`R$I%Ieo'Ifo(I)I*I+Icq,I{R|R-I.I[v]v/I:I;Iio=Ijo?I}R@Iyf[I{h]I~R^I_Ilo`Imo{I|I}I~IeqaJaSbSbJcJ^v_vdJeJfJpogJqohJcSiJAfjJ|hkJdSlJmJsonJtooJpJqJrJgqsJeSfStJuJ`v{vvJwJxJwoyJxozJgSAJCfBJ}hCJhSiSDJEJzoFJAoGJHJIJJJhqKJjSkSLJMJ|v}vNJOJPJDoQJEoRJlSSJEfTJ~hUJmSnSVJWJGoXJHoYJoSpS5sqSrSsStSuSvSwSxSySzSASBSCSDSESFSGSHSISJSKSLSMSNSOSPSQSRSSSTSUSVSWSXSYSZS0S1S2S3S6s7sTi4S5S6S7S8S9S!S#S$S%S'S(S)S*S8s9s!s#soV+S$s%s's(s,S-S.S/S:S;S=S$k?S@S[S]S^S_S`S{S|S}Smi~SaTbTcTdTeTfTgThTiTjTkTlTmTnToTpTqTrTsTtTuTvTwTxTyTzTATBTCTDTETFTGTHTITJTKTLTMTNTOTPTQTRTSTTTUTVTWTXTYTZT0T1T2T3T4T5T6T7T8T9T!T#T$T%T'T(T)T*T+T,T-T.T/T:T;T=T?T@T[T]T^T_T`TFfGfHfIfJfKfLfMfNfOfPfQfRfSfTfUfVfWfXfYfZf0f1f{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEU
103cdef CUresult cuCtxGetDevice(CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil:
104 return cydriver._cuCtxGetDevice(device) 2a kVlVPxN gbB *cM OiT U 4 v 7 w x y 5 z A J K L b c d e f g h i j k l m n o p q r s t u D E F G ezfzdimZCrAtgzBt%kVi'kWi(k)kNk#c7c8c9cVdO Zb$c%chbibjbPbkbV W X 6 QbRbSbpcmqnqoqOkPkQk4fRk*k+k4bXi4d5dYi,c6d!g#g$g%g=k?k5bZi7d8d0i-c9d'gSk(g)g{k1i|k2i}k~kal3ibl4icldlelfl6b5i!d#d6i.c$d*g+g,g-gmlnl7b7i%d'd8i/c(d.g/g:g;gulvl8b9i)d*d!i:c+d=g?g@g[gClDl9b#i,d-d$i;c.d]g^g_g`gKl%iLl'iMlNlOl(iPl)iQlRlSl*iTl+iUlVlSgpq+cIoONPNQNRNSNTNlbmbnbob0b1bTb5gWdPiqbrbXdQiqq8 H , - Ub2b3dVbI ~vrqawbwsqtqcwdwewfwgwhwiwjwkwuqlwmwnw,iowpwqwrwswvqtw7q8q9q!q#q$qhzizTgUg:JBwmVjzkzlzmz9r!rnzozpzqzrzsz#rtzuzvzwzxzyzzzAz$rBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z4z5z6z7z8z9z!z#z$z%z'z(z)z*z+z,z-z%r.z'r/z:z;z=z?z@z(r[z]z^z_z`z{z|z}z~zaAbAcAdAeAfAgAhAiA)rjAkA*rlAmAnAoApAqArAsAtAuAvAwA+rxAyAzAAABACADAEAFAGAHAIA,r-rJAKALAMA.rNAOAPAQARASATAUA/rVA:r.JbznVcz7rscQ tc;J0l=JZk0k1k2k3k4k5kRi6k6gqcEypboipi0dnZoZSiqirisitiui=cviwixiyi?cziAi@cBiCiDircEiFiGiHi[cIiJiKiLiMiCKppqppZrpsptpupvpwpxpypzpApBpCpDpEpFpGpHpIpJpKpLpMpNpOpPpQpRpSp;rTpWA=rYk1d2duwFU1l2lvwGUHUIU?rJUKU@r[rLUMU]r^rNUOUPU_rQU`rRUSUTUUU{rVU|r}rWUXUYUZU0U1U2U3U~rasbs4U5U6Ucs7Udsesfsgshs8Uis9U!Ujs#U$U%Uks'U(U)U*U+U,U-U.Uls/U:U;U=U?U@U[Umsns]U^U_U`Uos{U|U}U~UpsqsaVbVrssstscVusdVeVfVvsgVhViV9fki?dvbqZCtTkDt{g|g}gEt[ li]cUkrZ~g@d^c!bah[dbh]dch^ddh_d_c#beh`d!fXAucYA#fZA$f0A%f1A'f2Avc3A(f4Afh{d`c$bgh|dhh}dih~djhae{c%bkhlh)f*fmh|cwc}c3lNonhVkwb'b~c4lohphVNxb!c3byb2pHxCw5lwq6lpV7lqV8lC 9l9gxqyqzqAqBqCqDqEqDwFq!l#l$lwsxsUpVp5A%l6A'l7A(l8A)l9A*l!A+lFt,lGt-lHt.lIt/lJt:lKt;lLt=lMt?lNt@lOt[lPt]lQt^lRt_lSt`lTt{lUt|lVt}lWt~lsZamtZbm#Acm$Adm%Aem'Afm(Agm)Ahm*Aim+Ajm,Akm-Alm.Amm/Anm:Aom;Apm=Aqm?Arm@Asm[Atm]Aum^Avm_AwmuZxmrVymsVzmtVAmuVBmvVCmwVDmxVEmyVFmzVGmAVHmBVImCVJmDVKmEVLmFVMmGVNmOmTm(b/i=iXmbeceqh4p0m1m)b[i_i5mdeeerh6pzbfege`i+f,f-fadhesh.f/fie1 bdcdkeAbBbzc:f] ^ Cb9 ! # $ vh_ ;f@fAcid[f$m*b}ibj)mlemexh9pcjDbzhChgjjdkd]f-mjj` ldmdDhneoepeBcqe^fresekjEbFhGhqjndod_f/m{ pdqdBeCeDerd`fEeFe:m+btjwjGeHeKhLh,bagbgsdtdcgxjIeJeKeLeCcMeyjNeOe-bDcEcFcud.b/b| :b;b=b|m?bzjCjbnPeQeMh%pR FbGb@bGcHcIcJc% KcLcvdReSewdTeUeDj[bNhOhVeWePhdndgegfgenXexdggfnhgiggn]bEjHjYeZeQhRh} kgngVhMcNc0eJjnn^bLjOjrn1e2eYh*pHb3e4ePjogpgqgyd5eZhrgsg6e2 zdAd8eIbJbQctg~ abKb' ( ) * 2hbbugxgRcGdygyn_bSjVjCn9e!e4hJsFn`bXj0jJn#e$e5hKs1jcbHdId6h%e'e(eSc)ezg*e+e2jLb8h9h8jJdKdAg.pdbLdMd?e@e[eNdBg]e^eNn{b#j'j_e`e%h'h|bGgHgOdPdIg(j{e|e}e~eTcaf)jbfcf}bUcVcWcQd~bacebbcccdcYnec*j-j2ndfef(hNsS MbNbfcXcYcZc0c+ 1c2cRdffgfSdhfif5ngc.j/jJgKg:j;p)h*h+h6njfkf,h=p-h.h7nhc;j@jlfmfWk/hfbMgPg?h3c4cnf%nQsRs(nObof`j,npfqf]h^p_pSsTs/nic|jak?nrfsf^h|p]njcckfk{ntfuf_h~p~nkchkkkdovfwf`hbqgolcmkpkkoxfyf{hdqnomcrkukrozfAf|hfquoncwkzkyoBfCf}hZs0sBoocBkEkFoDfEf~h2s3sKxEK5sLxMxNx6s7sTi8s9s!s#soVOx$s%s's(s$kjVvZ%qEwFwGwHwIwmiJwKwLwMwNwOwPwQwRw7kSwPq'qTw7gUw)s*s+s,s-s.s/s:s;s=s?s@s[s]s^s_s`s{s|s}s~satbtctdtetftgthtitjtktltmtntotptqt`ArtstwZxZyZzZAZBZCZDZEZFZGZHZIZJZKZLZMZNZOZPZQZRZSZTZFfQqGfHfIfJfRqKfSqLfTqUqMfVqNfOfWqPfQfRfSfTfXqYqZq0qUfVfWfXf1q2q3qYfZf4q5q0f1fUZVZ
106cdef CUresult cuCtxGetDevice_v2(CUdevice* device, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
107 return cydriver._cuCtxGetDevice_v2(device, ctx)
109cdef CUresult cuCtxGetFlags(unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
110 return cydriver._cuCtxGetFlags(flags)
112cdef CUresult cuCtxSetFlags(unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
113 return cydriver._cuCtxSetFlags(flags)
115cdef CUresult cuCtxGetId(CUcontext ctx, unsigned long long* ctxId) except ?CUDA_ERROR_NOT_FOUND nogil:
116 return cydriver._cuCtxGetId(ctx, ctxId)
118cdef CUresult cuCtxSynchronize() except ?CUDA_ERROR_NOT_FOUND nogil:
119 return cydriver._cuCtxSynchronize()
121cdef CUresult cuCtxSynchronize_v2(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
122 return cydriver._cuCtxSynchronize_v2(ctx)
124cdef CUresult cuCtxSetLimit(CUlimit limit, size_t value) except ?CUDA_ERROR_NOT_FOUND nogil:
125 return cydriver._cuCtxSetLimit(limit, value)
127cdef CUresult cuCtxGetLimit(size_t* pvalue, CUlimit limit) except ?CUDA_ERROR_NOT_FOUND nogil:
128 return cydriver._cuCtxGetLimit(pvalue, limit)
130cdef CUresult cuCtxGetCacheConfig(CUfunc_cache* pconfig) except ?CUDA_ERROR_NOT_FOUND nogil:
131 return cydriver._cuCtxGetCacheConfig(pconfig)
133cdef CUresult cuCtxSetCacheConfig(CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
134 return cydriver._cuCtxSetCacheConfig(config)
136cdef CUresult cuCtxGetApiVersion(CUcontext ctx, unsigned int* version) except ?CUDA_ERROR_NOT_FOUND nogil:
137 return cydriver._cuCtxGetApiVersion(ctx, version)
139cdef CUresult cuCtxGetStreamPriorityRange(int* leastPriority, int* greatestPriority) except ?CUDA_ERROR_NOT_FOUND nogil:
140 return cydriver._cuCtxGetStreamPriorityRange(leastPriority, greatestPriority) 2N gbB *cM OiT U 4 WbXbYb'c(c)cv 7 w x y 5 z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G #c7c8c9cVdO Zb$c%chbibjbPbkbV W X 6 QbRbSbpc0b1bqbrbH , - 2b3dVbI P 3 FkGkHkIkJkKkLkMk8k?J@J6faiQgRg2f3fbici/ : ; = ? @ 7q8q9q!q#q$qBwscQ tcZk0k1k2k3k4k5kRi6k6gqcVgLoWgXgMoYgZg0gni1g2g3gXkpboipi0dSi1d2d(q)qSo*qTo+q,qUoVo-q.q/qWo:qXoYoZo0o1o2o3o4o5o;q6o7o8o9o=q!o#o?q@q[q]q$o^q%o_q`q'o(o{q|q}q)o~q*o+o,o-o.o/o:o;o=oar?o@o[o]obr^o_ocrdrerfr`ogr{ohrir|o}ojrkrlr~omrapbpcpdpepfpgphpipnrjpkplpmpornpopprqrvb[ nhwbC NiyszsAs!pRhjg} IjGskg'plgmgng(pShThUhVhMcHsNc0eJj)pWhXhIsLs/hLgfb[jOsMg?pNgOgPg@p:h;h=h?h3cPs4cnf%n[p@h[hTdUd`pUsVsWsXsYs1s4s%qEwFwGwHwIwmiJwKwLwMwNwOwPwQwRw7kSwPq'qTw7gUw
142cdef CUresult cuCtxResetPersistingL2Cache() except ?CUDA_ERROR_NOT_FOUND nogil:
143 return cydriver._cuCtxResetPersistingL2Cache()
145cdef CUresult cuCtxGetExecAffinity(CUexecAffinityParam* pExecAffinity, CUexecAffinityType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
146 return cydriver._cuCtxGetExecAffinity(pExecAffinity, typename)
148cdef CUresult cuCtxRecordEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
149 return cydriver._cuCtxRecordEvent(hCtx, hEvent)
151cdef CUresult cuCtxWaitEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
152 return cydriver._cuCtxWaitEvent(hCtx, hEvent)
154cdef CUresult cuCtxAttach(CUcontext* pctx, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
155 return cydriver._cuCtxAttach(pctx, flags)
157cdef CUresult cuCtxDetach(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
158 return cydriver._cuCtxDetach(ctx)
160cdef CUresult cuCtxGetSharedMemConfig(CUsharedconfig* pConfig) except ?CUDA_ERROR_NOT_FOUND nogil:
161 return cydriver._cuCtxGetSharedMemConfig(pConfig)
163cdef CUresult cuCtxSetSharedMemConfig(CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
164 return cydriver._cuCtxSetSharedMemConfig(config)
166cdef CUresult cuModuleLoad(CUmodule* module, const char* fname) except ?CUDA_ERROR_NOT_FOUND nogil:
167 return cydriver._cuModuleLoad(module, fname)
169cdef CUresult cuModuleLoadData(CUmodule* module, const void* image) except ?CUDA_ERROR_NOT_FOUND nogil:
170 return cydriver._cuModuleLoadData(module, image) 2YdZdeifigi5fhiii
172cdef CUresult cuModuleLoadDataEx(CUmodule* module, const void* image, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
173 return cydriver._cuModuleLoadDataEx(module, image, numOptions, options, optionValues) 2WZ
175cdef CUresult cuModuleLoadFatBinary(CUmodule* module, const void* fatCubin) except ?CUDA_ERROR_NOT_FOUND nogil:
176 return cydriver._cuModuleLoadFatBinary(module, fatCubin)
178cdef CUresult cuModuleUnload(CUmodule hmod) except ?CUDA_ERROR_NOT_FOUND nogil:
179 return cydriver._cuModuleUnload(hmod) 2YdZdeifigi5fhiii
181cdef CUresult cuModuleGetLoadingMode(CUmoduleLoadingMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
182 return cydriver._cuModuleGetLoadingMode(mode)
184cdef CUresult cuModuleGetFunction(CUfunction* hfunc, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
185 return cydriver._cuModuleGetFunction(hfunc, hmod, name) 2YdZdeifigi5fhiii
187cdef CUresult cuModuleGetFunctionCount(unsigned int* count, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
188 return cydriver._cuModuleGetFunctionCount(count, mod)
190cdef CUresult cuModuleEnumerateFunctions(CUfunction* functions, unsigned int numFunctions, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
191 return cydriver._cuModuleEnumerateFunctions(functions, numFunctions, mod)
193cdef CUresult cuModuleGetGlobal(CUdeviceptr* dptr, size_t* numbytes, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
194 return cydriver._cuModuleGetGlobal_v2(dptr, numbytes, hmod, name) 25f
196cdef CUresult cuLinkCreate(unsigned int numOptions, CUjit_option* options, void** optionValues, CUlinkState* stateOut) except ?CUDA_ERROR_NOT_FOUND nogil:
197 return cydriver._cuLinkCreate_v2(numOptions, options, optionValues, stateOut)
199cdef CUresult cuLinkAddData(CUlinkState state, CUjitInputType typename, void* data, size_t size, const char* name, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
200 return cydriver._cuLinkAddData_v2(state, typename, data, size, name, numOptions, options, optionValues)
202cdef CUresult cuLinkAddFile(CUlinkState state, CUjitInputType typename, const char* path, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
203 return cydriver._cuLinkAddFile_v2(state, typename, path, numOptions, options, optionValues)
205cdef CUresult cuLinkComplete(CUlinkState state, void** cubinOut, size_t* sizeOut) except ?CUDA_ERROR_NOT_FOUND nogil:
206 return cydriver._cuLinkComplete(state, cubinOut, sizeOut)
208cdef CUresult cuLinkDestroy(CUlinkState state) except ?CUDA_ERROR_NOT_FOUND nogil:
209 return cydriver._cuLinkDestroy(state)
211cdef CUresult cuModuleGetTexRef(CUtexref* pTexRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
212 return cydriver._cuModuleGetTexRef(pTexRef, hmod, name)
214cdef CUresult cuModuleGetSurfRef(CUsurfref* pSurfRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
215 return cydriver._cuModuleGetSurfRef(pSurfRef, hmod, name)
217cdef CUresult cuLibraryLoadData(CUlibrary* library, const void* code, CUjit_option* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, CUlibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?CUDA_ERROR_NOT_FOUND nogil:
218 return cydriver._cuLibraryLoadData(library, code, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2N gbB M T U 4 v 7 w x y 5 z A J K L b c d e f g h i j k l m n o p q r s t u D E F G O hbibjbPbkb4fRk4b,c5b-c6b.c7b/c8b:c9b;c+clbmbnbobTbqq8 H , - Ub3dVbI P 3 Q qcpb0dSiqirisitiui=cviwixiyi?cziAi@cBiCiDircEiFiGiHi[cIiJiKiLiMiCw5lwq6l7l8lC 9l9gxqyqzqAqBqCqDqEqDwFq!l#lHV$lXZ%l'l(l)l*l+l,l-l.l/l:l;l=l?l@l[l]l^l_l`l{l|l}l~lambmcmdmemfmgmhmimjmkmlmmmnmompmqmrmsmtmumvmwmxmymzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOm(bXmbe4p0m)b5mde6pzbad1 keAb:f] ^ Cb9 ! # $ _ Ac*b)mle9pDbgjjd-m` BcEbqjnd/m{ +bGeLh,bagbgsdtdcgxjIeJeKeLeCcMeyjNeOe-bDcEcFcud.b/b| :b;b=b?bbnPe%pR % Dj[bNhOhVeWePhdndgegfgenXexdggfnhgig]bYe} VhMcJj^brn1e*pHbyd2 8eIb~ abKb' ( ) * bbRc_bCn9e`bJn#ecbScLb8jJddb{b_e'h|bGgHgOdPdIg(j{e|e}e~eTcaf)jbfcf}bUcVcWcQd~bacebbcccdcec2ndfS + gc6njfhclffb?h3cOb,npf^p_pic?nrf|pjc{ntf~pkcdovfbqlckoxfdqmcrozffqncyoBfocFoDfTi
220cdef CUresult cuLibraryLoadFromFile(CUlibrary* library, const char* fileName, CUjit_option* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, CUlibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?CUDA_ERROR_NOT_FOUND nogil:
221 return cydriver._cuLibraryLoadFromFile(library, fileName, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2IV
223cdef CUresult cuLibraryUnload(CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
224 return cydriver._cuLibraryUnload(library)
226cdef CUresult cuLibraryGetKernel(CUkernel* pKernel, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
227 return cydriver._cuLibraryGetKernel(pKernel, library, name) 2N gbB M T U 4 v 7 w x y 5 z A J K L b c d e f g h i j k l m n o p q r s t u D E F G O hbibjbPbkb4fRk4b,c5b-c6b.c7b/c8b:c9b;c+clbmbnbobTbqq8 H , - Ub3dVbI P 3 Q qcpb0dSiqirisitiui=cviwixiyi?cziAi@cBiCiDircEiFiGiHi[cIiJiKiLiMiCw5lwq6l7l8lC 9l9gxqyqzqAqBqCqDqEqDwFq!lIV#lHV$l%l'l(l)l*l+l,l-l.l/l:l;l=l?l@l[l]l^l_l`l{l|l}l~lambmcmdmemfmgmhmimjmkmlmmmnmompmqmrmsmtmumvmwmxmymzmAmBmCmDmEmFmGmHmImJmKmLmMmNmOm(bXmbe0m)b5mdezbad1 keAb] ^ Cb9 ! # $ _ Ac*b)mleDbgjjd` BcEbqjnd{ +bGeLh,bagbgsdtdcgxjIeJeKeLeCcMeyjNeOe-bDcEcFcud.b/b| :b;b=b?bbnPeR % [benXe]bYe} VhMc^brn1eHbyd2 8eIb~ abKb' ( ) * bbRc_bCn9e`bJn#ecbScLb8jJddb{b_e'h|bGgHgOdPdIg(j{e|e}e~eTcaf)jbfcf}bUcVcWcQd~bacebbcccdcec2ndfS + gc6njfhclffb?h3cOb,npfic?nrfjc{ntfkcdovflckoxfmcrozfncyoBfocFoDfTi
229cdef CUresult cuLibraryGetKernelCount(unsigned int* count, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
230 return cydriver._cuLibraryGetKernelCount(count, lib)
232cdef CUresult cuLibraryEnumerateKernels(CUkernel* kernels, unsigned int numKernels, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
233 return cydriver._cuLibraryEnumerateKernels(kernels, numKernels, lib)
235cdef CUresult cuLibraryGetModule(CUmodule* pMod, CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
236 return cydriver._cuLibraryGetModule(pMod, library)
238cdef CUresult cuKernelGetFunction(CUfunction* pFunc, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
239 return cydriver._cuKernelGetFunction(pFunc, kernel)
241cdef CUresult cuKernelGetLibrary(CUlibrary* pLib, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
242 return cydriver._cuKernelGetLibrary(pLib, kernel)
244cdef CUresult cuLibraryGetGlobal(CUdeviceptr* dptr, size_t* numbytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
245 return cydriver._cuLibraryGetGlobal(dptr, numbytes, library, name)
247cdef CUresult cuLibraryGetManaged(CUdeviceptr* dptr, size_t* numbytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
248 return cydriver._cuLibraryGetManaged(dptr, numbytes, library, name)
250cdef CUresult cuLibraryGetUnifiedFunction(void** fptr, CUlibrary library, const char* symbol) except ?CUDA_ERROR_NOT_FOUND nogil:
251 return cydriver._cuLibraryGetUnifiedFunction(fptr, library, symbol)
253cdef CUresult cuKernelGetAttribute(int* pi, CUfunction_attribute attrib, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
254 return cydriver._cuKernelGetAttribute(pi, attrib, kernel, dev) 2qq8 H CwwqpVqVFtGtHtItJtKtLtMtNtOtPtQtRtStTtUtVtWtrVsVtVuVvVwVxVyVzVAVBVCVDVEVFVGV
256cdef CUresult cuKernelSetAttribute(CUfunction_attribute attrib, int val, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
257 return cydriver._cuKernelSetAttribute(attrib, val, kernel, dev)
259cdef CUresult cuKernelSetCacheConfig(CUkernel kernel, CUfunc_cache config, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
260 return cydriver._cuKernelSetCacheConfig(kernel, config, dev)
262cdef CUresult cuKernelGetName(const char** name, CUkernel hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
263 return cydriver._cuKernelGetName(name, hfunc) 2YZ
265cdef CUresult cuKernelGetParamInfo(CUkernel kernel, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil:
266 return cydriver._cuKernelGetParamInfo(kernel, paramIndex, paramOffset, paramSize) 2C 9gxqyqzqAqBqCqDqEqDwFqZZ
268cdef CUresult cuKernelGetParamCount(CUkernel kernel, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
269 return cydriver._cuKernelGetParamCount(kernel, paramCount)
271cdef CUresult cuMemGetInfo(size_t* free, size_t* total) except ?CUDA_ERROR_NOT_FOUND nogil:
272 return cydriver._cuMemGetInfo_v2(free, total)
274cdef CUresult cuMemAlloc(CUdeviceptr* dptr, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil:
275 return cydriver._cuMemAlloc_v2(dptr, bytesize) 2VwJV. KVLVMVNVOVPVQVRVSVTVUVYdZdYk1d2duwvw(q)qSo*qTo+q,qUoVo-q.q/qWo:qXoYoZo0o1o2o3o4o5o;q6o7o8o9o=q!o#o?q@q9f3lNonh
277cdef CUresult cuMemAllocPitch(CUdeviceptr* dptr, size_t* pPitch, size_t WidthInBytes, size_t Height, unsigned int ElementSizeBytes) except ?CUDA_ERROR_NOT_FOUND nogil:
278 return cydriver._cuMemAllocPitch_v2(dptr, pPitch, WidthInBytes, Height, ElementSizeBytes)
280cdef CUresult cuMemFree(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
281 return cydriver._cuMemFree_v2(dptr) 2v 7 w x y 5 z A J K L 8 / : ; = ? @ JoVwrrJV. KVLVMVNVOVPVQVRVSVTV7fpboipiUVYdZdYk1d2duw2lvwZpww(q)qSo*qTo+q,qUoVo-q.q/qWo:qXoYoZo0o1o2o3o4o5o;q6o7o8o9o=q!o#o?q@qerfr`ogr{ohrir|o}ojrkrlr~omrapbpcpdpepfpgphpipnrjpkplpmpornpopprqr9f3lNonhC
283cdef CUresult cuMemGetAddressRange(CUdeviceptr* pbase, size_t* psize, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
284 return cydriver._cuMemGetAddressRange_v2(pbase, psize, dptr)
286cdef CUresult cuMemAllocHost(void** pp, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil:
287 return cydriver._cuMemAllocHost_v2(pp, bytesize) 2N B U b c d e f g h i j k l m n o p q r s t u D E F G P 3 Q pbqirisitiui=cviwixiyi?cziAi@cBiCiDircEiFiGiHi[cIiJiKiLiMiYk1d2d1lxw0p[q]q$o^q%o_q`q'o(o{q|q}q)o~q*o+o,o-o.o/o:o;o=oar?o@o[o]obr^o_ocrdr9fC
289cdef CUresult cuMemFreeHost(void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
290 return cydriver._cuMemFreeHost(p) 2N B U b c d e f g h i j k l m n o p q r s t u D E F G VVWVQ pbqirisitiui=cviwixiyi?cziAi@cBiCiDircEiFiGiHi[cIiJiKiLiMiYk1d2d1lxw0p[q]q$o^q%o_q`q'o(o{q|q}q)o~q*o+o,o-o.o/o:o;o=oar?o@o[o]obr^o_ocrdr9fC
292cdef CUresult cuMemHostAlloc(void** pp, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
293 return cydriver._cuMemHostAlloc(pp, bytesize, Flags) 2VVWV
295cdef CUresult cuMemHostGetDevicePointer(CUdeviceptr* pdptr, void* p, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
296 return cydriver._cuMemHostGetDevicePointer_v2(pdptr, p, Flags)
298cdef CUresult cuMemHostGetFlags(unsigned int* pFlags, void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
299 return cydriver._cuMemHostGetFlags(pFlags, p)
301cdef CUresult cuMemAllocManaged(CUdeviceptr* dptr, size_t bytesize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
302 return cydriver._cuMemAllocManaged(dptr, bytesize, flags) 2v 7 w x y 5 z A J K L P 3 6faiQgRg2f3fbici/ : ; = ? @ JorrpboipiYk1d2d2lZpwwerfr`ogr{ohrir|o}ojrkrlr~omrapbpcpdpepfpgphpipnrjpkplpmpornpopprqr9f
304cdef CUresult cuDeviceRegisterAsyncNotification(CUdevice device, CUasyncCallback callbackFunc, void* userData, CUasyncCallbackHandle* callback) except ?CUDA_ERROR_NOT_FOUND nogil:
305 return cydriver._cuDeviceRegisterAsyncNotification(device, callbackFunc, userData, callback)
307cdef CUresult cuDeviceUnregisterAsyncNotification(CUdevice device, CUasyncCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
308 return cydriver._cuDeviceUnregisterAsyncNotification(device, callback)
310cdef CUresult cuDeviceGetByPCIBusId(CUdevice* dev, const char* pciBusId) except ?CUDA_ERROR_NOT_FOUND nogil:
311 return cydriver._cuDeviceGetByPCIBusId(dev, pciBusId)
313cdef CUresult cuDeviceGetPCIBusId(char* pciBusId, int length, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
314 return cydriver._cuDeviceGetPCIBusId(pciBusId, length, dev)
316cdef CUresult cuIpcGetEventHandle(CUipcEventHandle* pHandle, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
317 return cydriver._cuIpcGetEventHandle(pHandle, event) 2P 3 FkGkHkIkJkKkLkMk8kNiTdUd
319cdef CUresult cuIpcOpenEventHandle(CUevent* phEvent, CUipcEventHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
320 return cydriver._cuIpcOpenEventHandle(phEvent, handle)
322cdef CUresult cuIpcGetMemHandle(CUipcMemHandle* pHandle, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
323 return cydriver._cuIpcGetMemHandle(pHandle, dptr)
325cdef CUresult cuIpcOpenMemHandle(CUdeviceptr* pdptr, CUipcMemHandle handle, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
326 return cydriver._cuIpcOpenMemHandle_v2(pdptr, handle, Flags)
328cdef CUresult cuIpcCloseMemHandle(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
329 return cydriver._cuIpcCloseMemHandle(dptr)
331cdef CUresult cuMemHostRegister(void* p, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
332 return cydriver._cuMemHostRegister_v2(p, bytesize, Flags) 21pyw
334cdef CUresult cuMemHostUnregister(void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
335 return cydriver._cuMemHostUnregister(p) 21pyw
337cdef CUresult cuMemcpy(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
338 return cydriver._cuMemcpy(dst, src, ByteCount)
340cdef CUresult cuMemcpyPeer(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
341 return cydriver._cuMemcpyPeer(dstDevice, dstContext, srcDevice, srcContext, ByteCount)
343cdef CUresult cuMemcpyHtoD(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
344 return cydriver._cuMemcpyHtoD_v2(dstDevice, srcHost, ByteCount) 2Vw.
346cdef CUresult cuMemcpyDtoH(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
347 return cydriver._cuMemcpyDtoH_v2(dstHost, srcDevice, ByteCount) 2V W X 6 Vw.
349cdef CUresult cuMemcpyDtoD(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
350 return cydriver._cuMemcpyDtoD_v2(dstDevice, srcDevice, ByteCount)
352cdef CUresult cuMemcpyDtoA(CUarray dstArray, size_t dstOffset, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
353 return cydriver._cuMemcpyDtoA_v2(dstArray, dstOffset, srcDevice, ByteCount)
355cdef CUresult cuMemcpyAtoD(CUdeviceptr dstDevice, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
356 return cydriver._cuMemcpyAtoD_v2(dstDevice, srcArray, srcOffset, ByteCount)
358cdef CUresult cuMemcpyHtoA(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
359 return cydriver._cuMemcpyHtoA_v2(dstArray, dstOffset, srcHost, ByteCount)
361cdef CUresult cuMemcpyAtoH(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
362 return cydriver._cuMemcpyAtoH_v2(dstHost, srcArray, srcOffset, ByteCount)
364cdef CUresult cuMemcpyAtoA(CUarray dstArray, size_t dstOffset, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
365 return cydriver._cuMemcpyAtoA_v2(dstArray, dstOffset, srcArray, srcOffset, ByteCount)
367cdef CUresult cuMemcpy2D(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
368 return cydriver._cuMemcpy2D_v2(pCopy)
370cdef CUresult cuMemcpy2DUnaligned(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
371 return cydriver._cuMemcpy2DUnaligned_v2(pCopy)
373cdef CUresult cuMemcpy3D(const CUDA_MEMCPY3D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
374 return cydriver._cuMemcpy3D_v2(pCopy)
376cdef CUresult cuMemcpy3DPeer(const CUDA_MEMCPY3D_PEER* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
377 return cydriver._cuMemcpy3DPeer(pCopy)
379cdef CUresult cuMemcpyAsync(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
380 return cydriver._cuMemcpyAsync(dst, src, ByteCount, hStream) 2v 7 w x y 5 z A J K L P 3 6faiQgRg2f3fbici/ : ; = ? @ pboipi1d2dvb[ wbC
382cdef CUresult cuMemcpyPeerAsync(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
383 return cydriver._cuMemcpyPeerAsync(dstDevice, dstContext, srcDevice, srcContext, ByteCount, hStream)
385cdef CUresult cuMemcpyHtoDAsync(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
386 return cydriver._cuMemcpyHtoDAsync_v2(dstDevice, srcHost, ByteCount, hStream)
388cdef CUresult cuMemcpyDtoHAsync(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
389 return cydriver._cuMemcpyDtoHAsync_v2(dstHost, srcDevice, ByteCount, hStream) 2YdZd5f
391cdef CUresult cuMemcpyDtoDAsync(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
392 return cydriver._cuMemcpyDtoDAsync_v2(dstDevice, srcDevice, ByteCount, hStream)
394cdef CUresult cuMemcpyHtoAAsync(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
395 return cydriver._cuMemcpyHtoAAsync_v2(dstArray, dstOffset, srcHost, ByteCount, hStream)
397cdef CUresult cuMemcpyAtoHAsync(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
398 return cydriver._cuMemcpyAtoHAsync_v2(dstHost, srcArray, srcOffset, ByteCount, hStream)
400cdef CUresult cuMemcpy2DAsync(const CUDA_MEMCPY2D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
401 return cydriver._cuMemcpy2DAsync_v2(pCopy, hStream)
403cdef CUresult cuMemcpy3DAsync(const CUDA_MEMCPY3D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
404 return cydriver._cuMemcpy3DAsync_v2(pCopy, hStream)
406cdef CUresult cuMemcpy3DPeerAsync(const CUDA_MEMCPY3D_PEER* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
407 return cydriver._cuMemcpy3DPeerAsync(pCopy, hStream)
409cdef CUresult cuMemcpyBatchAsync(CUdeviceptr* dsts, CUdeviceptr* srcs, size_t* sizes, size_t count, CUmemcpyAttributes* attrs, size_t* attrsIdxs, size_t numAttrs, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
410 return cydriver._cuMemcpyBatchAsync_v2(dsts, srcs, sizes, count, attrs, attrsIdxs, numAttrs, hStream)
412cdef CUresult cuMemcpy3DBatchAsync(size_t numOps, CUDA_MEMCPY3D_BATCH_OP* opList, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
413 return cydriver._cuMemcpy3DBatchAsync_v2(numOps, opList, flags, hStream)
415cdef CUresult cuMemcpyWithAttributesAsync(CUdeviceptr dst, CUdeviceptr src, size_t size, CUmemcpyAttributes* attr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
416 return cydriver._cuMemcpyWithAttributesAsync(dst, src, size, attr, hStream)
418cdef CUresult cuMemcpy3DWithAttributesAsync(CUDA_MEMCPY3D_BATCH_OP* op, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
419 return cydriver._cuMemcpy3DWithAttributesAsync(op, flags, hStream)
421cdef CUresult cuMemsetD8(CUdeviceptr dstDevice, unsigned char uc, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
422 return cydriver._cuMemsetD8_v2(dstDevice, uc, N)
424cdef CUresult cuMemsetD16(CUdeviceptr dstDevice, unsigned short us, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
425 return cydriver._cuMemsetD16_v2(dstDevice, us, N)
427cdef CUresult cuMemsetD32(CUdeviceptr dstDevice, unsigned int ui, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
428 return cydriver._cuMemsetD32_v2(dstDevice, ui, N)
430cdef CUresult cuMemsetD2D8(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
431 return cydriver._cuMemsetD2D8_v2(dstDevice, dstPitch, uc, Width, Height)
433cdef CUresult cuMemsetD2D16(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
434 return cydriver._cuMemsetD2D16_v2(dstDevice, dstPitch, us, Width, Height)
436cdef CUresult cuMemsetD2D32(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
437 return cydriver._cuMemsetD2D32_v2(dstDevice, dstPitch, ui, Width, Height)
439cdef CUresult cuMemsetD8Async(CUdeviceptr dstDevice, unsigned char uc, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
440 return cydriver._cuMemsetD8Async(dstDevice, uc, N, hStream) 2v 7 w x SoVoXoYoZo6o7o$o(o*o+o,o?o@o`o}oapbpcpjpkp
442cdef CUresult cuMemsetD16Async(CUdeviceptr dstDevice, unsigned short us, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
443 return cydriver._cuMemsetD16Async(dstDevice, us, N, hStream) 2To0o1o2o8o9o%o-o.o/o[o]o{odpepfplpmp
445cdef CUresult cuMemsetD32Async(CUdeviceptr dstDevice, unsigned int ui, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
446 return cydriver._cuMemsetD32Async(dstDevice, ui, N, hStream) 2UoWo3o4o5o!o#o'o)o:o;o=o^o_o|o~ogphpipnpop
448cdef CUresult cuMemsetD2D8Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
449 return cydriver._cuMemsetD2D8Async(dstDevice, dstPitch, uc, Width, Height, hStream)
451cdef CUresult cuMemsetD2D16Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
452 return cydriver._cuMemsetD2D16Async(dstDevice, dstPitch, us, Width, Height, hStream)
454cdef CUresult cuMemsetD2D32Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
455 return cydriver._cuMemsetD2D32Async(dstDevice, dstPitch, ui, Width, Height, hStream)
457cdef CUresult cuArrayCreate(CUarray* pHandle, const CUDA_ARRAY_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
458 return cydriver._cuArrayCreate_v2(pHandle, pAllocateArray) 2XV
460cdef CUresult cuArrayGetDescriptor(CUDA_ARRAY_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
461 return cydriver._cuArrayGetDescriptor_v2(pArrayDescriptor, hArray)
463cdef CUresult cuArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUarray array) except ?CUDA_ERROR_NOT_FOUND nogil:
464 return cydriver._cuArrayGetSparseProperties(sparseProperties, array)
466cdef CUresult cuMipmappedArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUmipmappedArray mipmap) except ?CUDA_ERROR_NOT_FOUND nogil:
467 return cydriver._cuMipmappedArrayGetSparseProperties(sparseProperties, mipmap)
469cdef CUresult cuArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUarray array, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
470 return cydriver._cuArrayGetMemoryRequirements(memoryRequirements, array, device)
472cdef CUresult cuMipmappedArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUmipmappedArray mipmap, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
473 return cydriver._cuMipmappedArrayGetMemoryRequirements(memoryRequirements, mipmap, device)
475cdef CUresult cuArrayGetPlane(CUarray* pPlaneArray, CUarray hArray, unsigned int planeIdx) except ?CUDA_ERROR_NOT_FOUND nogil:
476 return cydriver._cuArrayGetPlane(pPlaneArray, hArray, planeIdx)
478cdef CUresult cuArrayDestroy(CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
479 return cydriver._cuArrayDestroy(hArray) 2XV
481cdef CUresult cuArray3DCreate(CUarray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
482 return cydriver._cuArray3DCreate_v2(pHandle, pAllocateArray)
484cdef CUresult cuArray3DGetDescriptor(CUDA_ARRAY3D_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
485 return cydriver._cuArray3DGetDescriptor_v2(pArrayDescriptor, hArray)
487cdef CUresult cuMipmappedArrayCreate(CUmipmappedArray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc, unsigned int numMipmapLevels) except ?CUDA_ERROR_NOT_FOUND nogil:
488 return cydriver._cuMipmappedArrayCreate(pHandle, pMipmappedArrayDesc, numMipmapLevels)
490cdef CUresult cuMipmappedArrayGetLevel(CUarray* pLevelArray, CUmipmappedArray hMipmappedArray, unsigned int level) except ?CUDA_ERROR_NOT_FOUND nogil:
491 return cydriver._cuMipmappedArrayGetLevel(pLevelArray, hMipmappedArray, level)
493cdef CUresult cuMipmappedArrayDestroy(CUmipmappedArray hMipmappedArray) except ?CUDA_ERROR_NOT_FOUND nogil:
494 return cydriver._cuMipmappedArrayDestroy(hMipmappedArray)
496cdef CUresult cuMemGetHandleForAddressRange(void* handle, CUdeviceptr dptr, size_t size, CUmemRangeHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
497 return cydriver._cuMemGetHandleForAddressRange(handle, dptr, size, handleType, flags)
499cdef CUresult cuMemBatchDecompressAsync(CUmemDecompressParams* paramsArray, size_t count, unsigned int flags, size_t* errorIndex, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
500 return cydriver._cuMemBatchDecompressAsync(paramsArray, count, flags, errorIndex, stream)
502cdef CUresult cuMemAddressReserve(CUdeviceptr* ptr, size_t size, size_t alignment, CUdeviceptr addr, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
503 return cydriver._cuMemAddressReserve(ptr, size, alignment, addr, flags) 2xb!c3byb
505cdef CUresult cuMemAddressFree(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
506 return cydriver._cuMemAddressFree(ptr, size) 2xb!c3byb
508cdef CUresult cuMemCreate(CUmemGenericAllocationHandle* handle, size_t size, const CUmemAllocationProp* prop, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
509 return cydriver._cuMemCreate(handle, size, prop, flags) 2xb!c3byb
511cdef CUresult cuMemRelease(CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
512 return cydriver._cuMemRelease(handle) 2xb!c3byb
514cdef CUresult cuMemMap(CUdeviceptr ptr, size_t size, size_t offset, CUmemGenericAllocationHandle handle, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
515 return cydriver._cuMemMap(ptr, size, offset, handle, flags) 2xb!c3byb
517cdef CUresult cuMemMapArrayAsync(CUarrayMapInfo* mapInfoList, unsigned int count, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
518 return cydriver._cuMemMapArrayAsync(mapInfoList, count, hStream)
520cdef CUresult cuMemUnmap(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
521 return cydriver._cuMemUnmap(ptr, size) 2xb!c3byb
523cdef CUresult cuMemSetAccess(CUdeviceptr ptr, size_t size, const CUmemAccessDesc* desc, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
524 return cydriver._cuMemSetAccess(ptr, size, desc, count) 2xb!c3byb
526cdef CUresult cuMemGetAccess(unsigned long long* flags, const CUmemLocation* location, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
527 return cydriver._cuMemGetAccess(flags, location, ptr)
529cdef CUresult cuMemExportToShareableHandle(void* shareableHandle, CUmemGenericAllocationHandle handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
530 return cydriver._cuMemExportToShareableHandle(shareableHandle, handle, handleType, flags)
532cdef CUresult cuMemImportFromShareableHandle(CUmemGenericAllocationHandle* handle, void* osHandle, CUmemAllocationHandleType shHandleType) except ?CUDA_ERROR_NOT_FOUND nogil:
533 return cydriver._cuMemImportFromShareableHandle(handle, osHandle, shHandleType)
535cdef CUresult cuMemGetAllocationGranularity(size_t* granularity, const CUmemAllocationProp* prop, CUmemAllocationGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil:
536 return cydriver._cuMemGetAllocationGranularity(granularity, prop, option) 2xb!c3byb
538cdef CUresult cuMemGetAllocationPropertiesFromHandle(CUmemAllocationProp* prop, CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
539 return cydriver._cuMemGetAllocationPropertiesFromHandle(prop, handle)
541cdef CUresult cuMemRetainAllocationHandle(CUmemGenericAllocationHandle* handle, void* addr) except ?CUDA_ERROR_NOT_FOUND nogil:
542 return cydriver._cuMemRetainAllocationHandle(handle, addr) 2xb!c3byb
544cdef CUresult cuMemFreeAsync(CUdeviceptr dptr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
545 return cydriver._cuMemFreeAsync(dptr, hStream) 2WbXbYb'c(c)cv 7 w x y 5 z A J K L sbtbubY Z 0 8 /d:dWliq;d=dWwXwYwZw0w1w2w3w4w5w6w7w/ : ; = ? @ TgUg7f8fjiki?dvbTk[ li]cUk^c!b_c#bucvc`c$b{c%b|cwc}c-iVkwb'b~cC {CnDqD)t*t+t,tGqHq-t.t/t:t;tRD=tSD?t@tTD[t]t^t%D]Dfu0uZF-u.u/u:uKqLq;u=u?u@u[u?F]u@F^u_u[F`u{u|ulGBGjv4v5c6c|HpIHIZI*I}IqJIJFfQqGfHfIfJfRqKfSqLfTqUqMfVqNfOfWqPfQfRfSfTfXqYqZq0qUfVfWfXf1q2q3qYfZf4q5q0f1fKo
547cdef CUresult cuMemAllocAsync(CUdeviceptr* dptr, size_t bytesize, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
548 return cydriver._cuMemAllocAsync(dptr, bytesize, hStream) 2'c(c)cv w x y z A J K L sbtbubY Z 0
550cdef CUresult cuMemPoolTrimTo(CUmemoryPool pool, size_t minBytesToKeep) except ?CUDA_ERROR_NOT_FOUND nogil:
551 return cydriver._cuMemPoolTrimTo(pool, minBytesToKeep)
553cdef CUresult cuMemPoolSetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
554 return cydriver._cuMemPoolSetAttribute(pool, attr, value) 28wtg
556cdef CUresult cuMemPoolGetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
557 return cydriver._cuMemPoolGetAttribute(pool, attr, value) 2WbXbYbv 7 w x y 5 z A 8wTgUg8fjiki?dli~g@d^c!bah[dbh]dch^ddh_d_c#beh`d!fuc#f$f%f'fvc(ffh{d`c$bgh|dhh}dih~djhae{c%bkhlh)f*fmh|cwc}cC .i?i@iie1 jebdxcyccdthddedfdkeAb{iBbzc:fuhgdhd|iyhEhjgKj6e2 7ezdOcPcAd0hBdCdDd8eIbQjJbQctg1hEdFdRjWj7hLg]j{jbkgklkqkvkAkFfGfHfIfJfKfLfMfNfOfPfQfRfSfTfUfVfWfXfYfZf0f1fKo
559cdef CUresult cuMemPoolSetAccess(CUmemoryPool pool, const CUmemAccessDesc* map, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
560 return cydriver._cuMemPoolSetAccess(pool, map, count) 28 /d:d;d=deyfygyhyiyjykylymynyoypyqyrysytyuyvywyxyyyzyAyByCyDy/ : ; = ? @ 7fvb{g|g}g[ ]c~g@d^c!bah[dbh]dch^ddh_d_c#beh`d!fuc#f$f%f'fvc(ffh{d`c$bgh|dhh}dih~djhae{c%bkhlh)f*fmh|cwc}c-iwb'b~c4lohphC PmQmRmSm5c6c
562cdef CUresult cuMemPoolGetAccess(CUmemAccess_flags* flags, CUmemoryPool memPool, CUmemLocation* location) except ?CUDA_ERROR_NOT_FOUND nogil:
563 return cydriver._cuMemPoolGetAccess(flags, memPool, location)
565cdef CUresult cuMemPoolCreate(CUmemoryPool* pool, const CUmemPoolProps* poolProps) except ?CUDA_ERROR_NOT_FOUND nogil:
566 return cydriver._cuMemPoolCreate(pool, poolProps) 2ZJ~v/dkq:drq0Jaw;d1J=dbwXlsqZltq2Jcw3J4J5J#k6J7J8J9J!J#J$J%Jdwewfwgwhwiwjwkwuqlwmwnw'J,i(Jow)Jpw*Jqw+Jrw2f3f,Jswlqvq-Jtw/ : ; = ? @ 8wvb{g|g}g[ ]c~g@d^c!bah[dbh]dch^ddh_d_c#beh`d!fuc#f$f%f'fvc(ffh{d`c$bgh|dhh}dih~djhae{c%bkhlh)f*fmh|cwc}c-iwb'b~c4lohphPmQmRmSm5c6c
568cdef CUresult cuMemPoolDestroy(CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
569 return cydriver._cuMemPoolDestroy(pool) 28 /d:d;d=deyfygyhyiyjykylymynyoypyqyrysytyuyvywyxyyyzyAyByCyDy/ : ; = ? @ 8w7fvb{g|g}g[ ]c~g@d^c!bah[dbh]dch^ddh_d_c#beh`d!fuc#f$f%f'fvc(ffh{d`c$bgh|dhh}dih~djhae{c%bkhlh)f*fmh|cwc}c-iwb'b~c4lohphC PmQmRmSm5c6c
571cdef CUresult cuMemGetDefaultMemPool(CUmemoryPool* pool_out, CUmemLocation* location, CUmemAllocationType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
572 return cydriver._cuMemGetDefaultMemPool(pool_out, location, typename)
574cdef CUresult cuMemGetMemPool(CUmemoryPool* pool, CUmemLocation* location, CUmemAllocationType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
575 return cydriver._cuMemGetMemPool(pool, location, typename) 2CtTkDt{g|g}gEt[ ]cUk!fXAucYA#fZA$f0A%f1A'f2Avc3A(f4A*fwcVk
577cdef CUresult cuMemSetMemPool(CUmemLocation* location, CUmemAllocationType typename, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
578 return cydriver._cuMemSetMemPool(location, typename, pool)
580cdef CUresult cuMemAllocFromPoolAsync(CUdeviceptr* dptr, size_t bytesize, CUmemoryPool pool, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
581 return cydriver._cuMemAllocFromPoolAsync(dptr, bytesize, pool, hStream) 2WbXbYbv 7 w x y 5 z A /d:dWliq;d=dP 3 YljqWwXwYwZw0w1w2w3w4w5w6w7wWpttutvtXpwt6faiQgRg2f3fbicixtytYpzt/ : ; = ? @ TgUg8fjiki?dvbTk[ li]cUk^c!b_c#bucvc`c$b{c%b|cwc}c-iVkwb'b~cC .i?i@iie1 jebdxcyccdthddedfdkeAb{iBbzc:fuhgdhd|iyhEhjgKj6e2 7ezdOcPcAd0hBdCdDd8eIbQjJbQctg1hEdFdRjWj7hLg5c6c]j{jbkgklkqkvkAkFfQqGfHfIfJfRqKfSqLfTqUqMfVqNfOfWqPfQfRfSfTfXqYqZq0qUfVfWfXf1q2q3qYfZf4q5q0f1fKo
583cdef CUresult cuMemPoolExportToShareableHandle(void* handle_out, CUmemoryPool pool, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
584 return cydriver._cuMemPoolExportToShareableHandle(handle_out, pool, handleType, flags) 2ZJ~v/dkq:drq0Jaw;d1J=dbwXlsqZltq2Jcw3J4J5J#k6J7J8J9J!J#J$J%Jdwewfwgwhwiwjwkwuqlwmwnw'J,i(Jow)Jpw*Jqw+Jrw2f3f,Jswlqvq-Jtw/ : ; = ? @ @d!b[d]d^d_d#b`d{d$b|d}d~dae%blh'bohphPmQmRmSm5c6c
586cdef CUresult cuMemPoolImportFromShareableHandle(CUmemoryPool* pool_out, void* handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
587 return cydriver._cuMemPoolImportFromShareableHandle(pool_out, handle, handleType, flags)
589cdef CUresult cuMemPoolExportPointer(CUmemPoolPtrExportData* shareData_out, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
590 return cydriver._cuMemPoolExportPointer(shareData_out, ptr) 2/d:dWliq;d=dP 3 YljqWwXwYwZw0w1w2w3w4w5w6w7wWpttutvtXpwt6faiQgRg2f3fbicixtytYpzt/ : ; = ? @ 'b5c6c
592cdef CUresult cuMemPoolImportPointer(CUdeviceptr* ptr_out, CUmemoryPool pool, CUmemPoolPtrExportData* shareData) except ?CUDA_ERROR_NOT_FOUND nogil:
593 return cydriver._cuMemPoolImportPointer(ptr_out, pool, shareData)
595cdef CUresult cuMulticastCreate(CUmemGenericAllocationHandle* mcHandle, const CUmulticastObjectProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
596 return cydriver._cuMulticastCreate(mcHandle, prop)
598cdef CUresult cuMulticastAddDevice(CUmemGenericAllocationHandle mcHandle, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
599 return cydriver._cuMulticastAddDevice(mcHandle, dev)
601cdef CUresult cuMulticastBindMem(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUmemGenericAllocationHandle memHandle, size_t memOffset, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
602 return cydriver._cuMulticastBindMem(mcHandle, mcOffset, memHandle, memOffset, size, flags)
604cdef CUresult cuMulticastBindMem_v2(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, CUmemGenericAllocationHandle memHandle, size_t memOffset, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
605 return cydriver._cuMulticastBindMem_v2(mcHandle, dev, mcOffset, memHandle, memOffset, size, flags)
607cdef CUresult cuMulticastBindAddr(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
608 return cydriver._cuMulticastBindAddr(mcHandle, mcOffset, memptr, size, flags)
610cdef CUresult cuMulticastBindAddr_v2(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
611 return cydriver._cuMulticastBindAddr_v2(mcHandle, dev, mcOffset, memptr, size, flags)
613cdef CUresult cuMulticastUnbind(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
614 return cydriver._cuMulticastUnbind(mcHandle, dev, mcOffset, size)
616cdef CUresult cuMulticastGetGranularity(size_t* granularity, const CUmulticastObjectProp* prop, CUmulticastGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil:
617 return cydriver._cuMulticastGetGranularity(granularity, prop, option)
619cdef CUresult cuPointerGetAttribute(void* data, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
620 return cydriver._cuPointerGetAttribute(data, attribute, ptr) 2V W X 6 6d9d$d(d+d.drrceeeheBbidmekdqeodrdHeCc| QeR FbGb@bGcHcIcJcwdxdZeNc2e5eJbGd!e$e)eKdNd`eTcebefS MbNbfcXcYcZc0cSdkfmf4cqfsfufwfyfAfCfEf
622cdef CUresult cuMemPrefetchAsync(CUdeviceptr devPtr, size_t count, CUmemLocation location, unsigned int flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
623 return cydriver._cuMemPrefetchAsync_v2(devPtr, count, location, flags, hStream)
625cdef CUresult cuMemAdvise(CUdeviceptr devPtr, size_t count, CUmem_advise advice, CUmemLocation location) except ?CUDA_ERROR_NOT_FOUND nogil:
626 return cydriver._cuMemAdvise_v2(devPtr, count, advice, location) 2Jo
628cdef CUresult cuMemPrefetchBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, CUmemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
629 return cydriver._cuMemPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream)
631cdef CUresult cuMemDiscardBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
632 return cydriver._cuMemDiscardBatchAsync(dptrs, sizes, count, flags, hStream)
634cdef CUresult cuMemDiscardAndPrefetchBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, CUmemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
635 return cydriver._cuMemDiscardAndPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream)
637cdef CUresult cuMemRangeGetAttribute(void* data, size_t dataSize, CUmem_range_attribute attribute, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
638 return cydriver._cuMemRangeGetAttribute(data, dataSize, attribute, devPtr, count) 2Jo
640cdef CUresult cuMemRangeGetAttributes(void** data, size_t* dataSizes, CUmem_range_attribute* attributes, size_t numAttributes, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
641 return cydriver._cuMemRangeGetAttributes(data, dataSizes, attributes, numAttributes, devPtr, count) 2Jo
643cdef CUresult cuPointerSetAttribute(const void* value, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
644 return cydriver._cuPointerSetAttribute(value, attribute, ptr) 2rr
646cdef CUresult cuPointerGetAttributes(unsigned int numAttributes, CUpointer_attribute* attributes, void** data, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
647 return cydriver._cuPointerGetAttributes(numAttributes, attributes, data, ptr) 2rr0Z8fji1ZZpwwxw0p1pyw2Z3Z4Z5Z6Z7Z
649cdef CUresult cuStreamCreate(CUstream* phStream, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
650 return cydriver._cuStreamCreate(phStream, Flags) 28g. YVYdZdeifigi5fhiii
652cdef CUresult cuStreamCreateWithPriority(CUstream* phStream, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil:
653 return cydriver._cuStreamCreateWithPriority(phStream, flags, priority) 2N gbB *cM OiT U 4 WbXbYb'c(c)cv 7 w x y 5 z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G #c7c8c9cVdO Zb$c%chbibjbPbkbV W X 6 QbRbSbpc0b1bqbrbH , - 2b3dVbI P 3 FkGkHkIkJkKkLkMk8k?J@J6faiQgRg2f3fbici/ : ; = ? @ 7q8q9q!q#q$qBwscQ tcZk0k1k2k3k4k5kRi6k6gqcVgLoWgXgMoYgZg0gni1g2g3gXkpboipi0dSi1d2d(q)qSo*qTo+q,qUoVo-q.q/qWo:qXoYoZo0o1o2o3o4o5o;q6o7o8o9o=q!o#o?q@q[q]q$o^q%o_q`q'o(o{q|q}q)o~q*o+o,o-o.o/o:o;o=oar?o@o[o]obr^o_ocrdrerfr`ogr{ohrir|o}ojrkrlr~omrapbpcpdpepfpgphpipnrjpkplpmpornpopprqrvb[ nhwbC NiyszsAs!pRhjg} IjGskg'plgmgng(pShThUhVhMcHsNc0eJj)pWhXhIsLs/hLgfb[jOsMg?pNgOgPg@p:h;h=h?h3cPs4cnf%n[p@h[hTdUd`pUsVsWsXsYs1s4s%qEwFwGwHwIwmiJwKwLwMwNwOwPwQwRw7kSwPq'qTw7gUw
655cdef CUresult cuStreamBeginCaptureToCig(CUstream hStream, CUstreamCigCaptureParams* streamCigCaptureParams) except ?CUDA_ERROR_NOT_FOUND nogil:
656 return cydriver._cuStreamBeginCaptureToCig(hStream, streamCigCaptureParams)
658cdef CUresult cuStreamEndCaptureToCig(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
659 return cydriver._cuStreamEndCaptureToCig(hStream)
661cdef CUresult cuStreamGetPriority(CUstream hStream, int* priority) except ?CUDA_ERROR_NOT_FOUND nogil:
662 return cydriver._cuStreamGetPriority(hStream, priority)
664cdef CUresult cuStreamGetDevice(CUstream hStream, CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil:
665 return cydriver._cuStreamGetDevice(hStream, device)
667cdef CUresult cuStreamGetFlags(CUstream hStream, unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
668 return cydriver._cuStreamGetFlags(hStream, flags)
670cdef CUresult cuStreamGetId(CUstream hStream, unsigned long long* streamId) except ?CUDA_ERROR_NOT_FOUND nogil:
671 return cydriver._cuStreamGetId(hStream, streamId)
673cdef CUresult cuStreamGetCtx(CUstream hStream, CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
674 return cydriver._cuStreamGetCtx(hStream, pctx) 2B b c d e f g h i j k l m n o p q r s t u D E F G I P 3 FkGkHkIkJkKkLkMk7q8q9q!q#q$q`p%qmi
676cdef CUresult cuStreamGetCtx_v2(CUstream hStream, CUcontext* pCtx, CUgreenCtx* pGreenCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
677 return cydriver._cuStreamGetCtx_v2(hStream, pCtx, pGreenCtx)
679cdef CUresult cuStreamWaitEvent(CUstream hStream, CUevent hEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
680 return cydriver._cuStreamWaitEvent(hStream, hEvent, Flags) 2M T b c d e f g h i j k l m n o p q r s t u I 7g
682cdef CUresult cuStreamAddCallback(CUstream hStream, CUstreamCallback callback, void* userData, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
683 return cydriver._cuStreamAddCallback(hStream, callback, userData, flags)
685cdef CUresult cuStreamBeginCapture(CUstream hStream, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil:
686 return cydriver._cuStreamBeginCapture_v2(hStream, mode) 2N gbB *cM OiT U 4 WbXbYb'c(c)cv w x y z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G 3dVbI
688cdef CUresult cuStreamBeginCaptureToGraph(CUstream hStream, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil:
689 return cydriver._cuStreamBeginCaptureToGraph(hStream, hGraph, dependencies, dependencyData, numDependencies, mode) 1BbcdefghijklmnopqrstuDEFGI
691cdef CUresult cuThreadExchangeStreamCaptureMode(CUstreamCaptureMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
692 return cydriver._cuThreadExchangeStreamCaptureMode(mode)
694cdef CUresult cuStreamEndCapture(CUstream hStream, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
695 return cydriver._cuStreamEndCapture(hStream, phGraph) 2N gbB *cM OiT U 4 WbXbYb'c(c)cv w x y z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G 3dVbI
697cdef CUresult cuStreamIsCapturing(CUstream hStream, CUstreamCaptureStatus* captureStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
698 return cydriver._cuStreamIsCapturing(hStream, captureStatus) 2WbXbYb'c(c)cv 7 w x y 5 z A J K L sbtbubY Z 0 /d:dWliq;d=dP 3 YljqWwXwYwZw0w1w2w3w4w5w6w7wWpttutvtXpwt6faiQgRg2f3fbicixtytYpzt/ : ; = ? @ TgUg8fjiki?dvbTk[ li]cUk^c!b_c#bucvc`c$b{c%b|cwc}c-iVkwb'b~cC .i?i@iie1 jebdxcyccdthddedfdkeAb{iBbzc:fuhgdhd|iyhEhjgKj6e2 7ezdOcPcAd0hBdCdDd8eIbQjJbQctg1hEdFdRjWj7hLg5c6c]j{jbkgklkqkvkAkFfQqGfHfIfJfRqKfSqLfTqUqMfVqNfOfWqPfQfRfSfTfXqYqZq0qUfVfWfXf1q2q3qYfZf4q5q0f1fKo
700cdef CUresult cuStreamGetCaptureInfo(CUstream hStream, CUstreamCaptureStatus* captureStatus_out, cuuint64_t* id_out, CUgraph* graph_out, const CUgraphNode** dependencies_out, const CUgraphEdgeData** edgeData_out, size_t* numDependencies_out) except ?CUDA_ERROR_NOT_FOUND nogil:
701 return cydriver._cuStreamGetCaptureInfo_v3(hStream, captureStatus_out, id_out, graph_out, dependencies_out, edgeData_out, numDependencies_out) 2N gbB *cM OiT U 4 WbXbYb'c(c)cv w x y z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G 3dVbI
703cdef CUresult cuStreamUpdateCaptureDependencies(CUstream hStream, CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
704 return cydriver._cuStreamUpdateCaptureDependencies_v2(hStream, dependencies, dependencyData, numDependencies, flags) 1NBbcdefghijklmnopqrstuDEFGI
706cdef CUresult cuStreamAttachMemAsync(CUstream hStream, CUdeviceptr dptr, size_t length, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
707 return cydriver._cuStreamAttachMemAsync(hStream, dptr, length, flags)
709cdef CUresult cuStreamQuery(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
710 return cydriver._cuStreamQuery(hStream)
712cdef CUresult cuStreamSynchronize(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
713 return cydriver._cuStreamSynchronize(hStream) 2N gbB M U 4 v 7 w x y 5 z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G #c7c8c9cVdO Zb$c%chbibjbPbkbV W X 6 QbRbSbpc0b1bqbrbH , - 2b. sctcpbYdZdeifigi5fhiii0dSiqirisitiui=cviwixiyi?cziAi@cBiCiDircEiFiGiHi[cIiJiKiLiMiC 'q7g
715cdef CUresult cuStreamDestroy(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
716 return cydriver._cuStreamDestroy_v2(hStream) 28ZN gbB *cM OiT U 4 WbXbYb'c(c)cv 7 w x y 5 z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G #c7c8c9cVdO Zb$c%chbibjbPbkbV W X 6 QbRbSbpc0b1bqbrb8 H , - 2b3dVbI 8k?J@J/ : ; = ? @ 7q8q9q!q#q$q8g. BwscQ tcZk0k1k2k3k4k5kRi6k6gqcVgWgXgMoYgZg0g1g2g3g7fpboipiYVYdZdeifigi5fhiii0dSi1d2d(q)qSo*qTo+q,qUoVo-q.q/qWo:qXoYoZo0o1o2o3o4o5o;q6o7o8o9o=q!o#o?q@q[q]q$o^q%o_q`q'o(o{q|q}q)o~q*o+o,o-o.o/o:o;o=oar?o@o[o]obr^o_ocrdrerfr`ogr{ohrir|o}ojrkrlr~omrapbpcpdpepfpgphpipnrjpkplpmpornpopprqrvb[ NowbC NikDoDEDgEZu0u1u2uTF3u4uIqJq5u6u7u8u9uUF!uVF#u$uWF%u'u(u%FPG3v4v5v6v[H7v8vMqNq9v!v#v$v%v]H'v^H(v)v_H*v+v,vTdUdlIDIVI%I_ImJEJWJ%qEwFwGwHwIwmiJwKwLwMwNwOwPwQwRw7kSwPq'qTw7gUw
718cdef CUresult cuStreamCopyAttributes(CUstream dst, CUstream src) except ?CUDA_ERROR_NOT_FOUND nogil:
719 return cydriver._cuStreamCopyAttributes(dst, src)
721cdef CUresult cuStreamGetAttribute(CUstream hStream, CUstreamAttrID attr, CUstreamAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
722 return cydriver._cuStreamGetAttribute(hStream, attr, value_out)
724cdef CUresult cuStreamSetAttribute(CUstream hStream, CUstreamAttrID attr, const CUstreamAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
725 return cydriver._cuStreamSetAttribute(hStream, attr, value)
727cdef CUresult cuEventCreate(CUevent* phEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
728 return cydriver._cuEventCreate(phEvent, Flags) 2M T b c d e f g h i j k l m n o p q r s t u Zb4d5d7d8d!d#d%d'd)d*d,d-d5gWdPiqbrbXdQiH I P 3 FkGkHkIkJkKkLkMk8k:JscQ tc;J0l=JZk0k1k2k3k4k5kRi6k6gqcZVNiGy:i;iKy]i^ifegexcyc] ^ =f?f~iajBsAhBhldmdkjEhEb.mRyFhljmjGhEsnjojpjqjndSyod_f/mFsrjsjHhIhteueveweJhxeyezeAepdqdujvjsdtdDcEcAjBjFbGbKcLcVeWeFjGj'plgmgWyMjNj3e4eOcPc~ abvgwgTjUj1yYjZjHdId2j7hLbMn4y8h3j4j9h/J5j6j7j8jJd5yKdAg.pMs9j!j!h#h4g,e-e.e$h/e:e;e=eLdMd$j%jOdPdUcVc+j,jMbNb1c2cJgKg=j?j?pNgOgTdUd!y^j_j%y}j~j*ydkek.yikjk=ynkok]ysktk`yxkyk}yCkDk7k7g
730cdef CUresult cuEventRecord(CUevent hEvent, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
731 return cydriver._cuEventRecord(hEvent, hStream) 2M T b c d e f g h i j k l m n o p q r s t u I P 3 FkGkHkIkJkKkLkMk8kscQ tcZk0k1k2k3k4k5kRi6k6gqcNiTdUd7k7g
733cdef CUresult cuEventRecordWithFlags(CUevent hEvent, CUstream hStream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
734 return cydriver._cuEventRecordWithFlags(hEvent, hStream, flags)
736cdef CUresult cuEventQuery(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
737 return cydriver._cuEventQuery(hEvent) 25gWdXdRi6g
739cdef CUresult cuEventSynchronize(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
740 return cydriver._cuEventSynchronize(hEvent) 2Q 6gqc
742cdef CUresult cuEventDestroy(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
743 return cydriver._cuEventDestroy_v2(hEvent) 2M T b c d e f g h i j k l m n o p q r s t u XtYtZt0t1t2t3t4t5t6t7t8t9t5gWdPiXdQiI 8k:JscQ tc;J0l=JZk0k1k2k3k4k5kRi6k6gqcZVC NiaD!t#tuD$t%t't(tGqHq_t`t{t|t}t~t{DaubucudueufuguhuuEiujukulumunuoupuvEquwErusuxEtuuuvuwuxuyuzuAuBuCuDuEuFuGuHuIuJuKuLuMuNuOuPuQuRuSuTuUuVuWuXuYu4uIqJq3F)u*u+u,uKqLq}u~uavbvcvdvFGevfvgvhvivjvkvlv3Gmvnvovpvqvrvsvtv4Guv5Gvvwv6GxvyvzvAvBvCvDvEvFvGvHvIvJvKvLvMvNvOvPvQvRvSvTvUvVvWvXvYvZv0v1v2v8vMqNqTdUdbI-v.vtI/v:vLI;v=v3I?v@v.I[v]vcJ^v_vuJ`v{vMJ|v}v7k7g
745cdef CUresult cuEventElapsedTime(float* pMilliseconds, CUevent hStart, CUevent hEnd) except ?CUDA_ERROR_NOT_FOUND nogil:
746 return cydriver._cuEventElapsedTime_v2(pMilliseconds, hStart, hEnd) 2scQ tcqc
748cdef CUresult cuImportExternalMemory(CUexternalMemory* extMem_out, const CUDA_EXTERNAL_MEMORY_HANDLE_DESC* memHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
749 return cydriver._cuImportExternalMemory(extMem_out, memHandleDesc)
751cdef CUresult cuExternalMemoryGetMappedBuffer(CUdeviceptr* devPtr, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_BUFFER_DESC* bufferDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
752 return cydriver._cuExternalMemoryGetMappedBuffer(devPtr, extMem, bufferDesc)
754cdef CUresult cuExternalMemoryGetMappedMipmappedArray(CUmipmappedArray* mipmap, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC* mipmapDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
755 return cydriver._cuExternalMemoryGetMappedMipmappedArray(mipmap, extMem, mipmapDesc)
757cdef CUresult cuDestroyExternalMemory(CUexternalMemory extMem) except ?CUDA_ERROR_NOT_FOUND nogil:
758 return cydriver._cuDestroyExternalMemory(extMem)
760cdef CUresult cuImportExternalSemaphore(CUexternalSemaphore* extSem_out, const CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC* semHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
761 return cydriver._cuImportExternalSemaphore(extSem_out, semHandleDesc)
763cdef CUresult cuSignalExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
764 return cydriver._cuSignalExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream)
766cdef CUresult cuWaitExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
767 return cydriver._cuWaitExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream)
769cdef CUresult cuDestroyExternalSemaphore(CUexternalSemaphore extSem) except ?CUDA_ERROR_NOT_FOUND nogil:
770 return cydriver._cuDestroyExternalSemaphore(extSem)
772cdef CUresult cuStreamWaitValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
773 return cydriver._cuStreamWaitValue32_v2(stream, addr, value, flags)
775cdef CUresult cuStreamWaitValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
776 return cydriver._cuStreamWaitValue64_v2(stream, addr, value, flags)
778cdef CUresult cuStreamWriteValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
779 return cydriver._cuStreamWriteValue32_v2(stream, addr, value, flags)
781cdef CUresult cuStreamWriteValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
782 return cydriver._cuStreamWriteValue64_v2(stream, addr, value, flags)
784cdef CUresult cuStreamBatchMemOp(CUstream stream, unsigned int count, CUstreamBatchMemOpParams* paramArray, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
785 return cydriver._cuStreamBatchMemOp_v2(stream, count, paramArray, flags)
787cdef CUresult cuFuncGetAttribute(int* pi, CUfunction_attribute attrib, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
788 return cydriver._cuFuncGetAttribute(pi, attrib, hfunc)
790cdef CUresult cuFuncSetAttribute(CUfunction hfunc, CUfunction_attribute attrib, int value) except ?CUDA_ERROR_NOT_FOUND nogil:
791 return cydriver._cuFuncSetAttribute(hfunc, attrib, value)
793cdef CUresult cuFuncSetCacheConfig(CUfunction hfunc, CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
794 return cydriver._cuFuncSetCacheConfig(hfunc, config)
796cdef CUresult cuFuncGetModule(CUmodule* hmod, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
797 return cydriver._cuFuncGetModule(hmod, hfunc)
799cdef CUresult cuFuncGetName(const char** name, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
800 return cydriver._cuFuncGetName(name, hfunc) 29Z
802cdef CUresult cuFuncGetParamInfo(CUfunction func, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil:
803 return cydriver._cuFuncGetParamInfo(func, paramIndex, paramOffset, paramSize)
805cdef CUresult cuFuncGetParamCount(CUfunction func, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
806 return cydriver._cuFuncGetParamCount(func, paramCount)
808cdef CUresult cuFuncIsLoaded(CUfunctionLoadingState* state, CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
809 return cydriver._cuFuncIsLoaded(state, function)
811cdef CUresult cuFuncLoad(CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
812 return cydriver._cuFuncLoad(function)
814cdef CUresult cuLaunchKernel(CUfunction f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, CUstream hStream, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil:
815 return cydriver._cuLaunchKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams, extra) 2YdZdeifigi5fhiii
817cdef CUresult cuLaunchKernelEx(const CUlaunchConfig* config, CUfunction f, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil:
818 return cydriver._cuLaunchKernelEx(config, f, kernelParams, extra) 2N gbB M T U 4 v 7 w x y 5 z A J K L b c d e f g h i j k l m n o p q r s t u D E F G 3dVbI P 3 Q qcpb0dSiqirisitiui=cviwixiyi?cziAi@cBiCiDircEiFiGiHi[cIiJiKiLiMiC
820cdef CUresult cuLaunchCooperativeKernel(CUfunction f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, CUstream hStream, void** kernelParams) except ?CUDA_ERROR_NOT_FOUND nogil:
821 return cydriver._cuLaunchCooperativeKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams)
823cdef CUresult cuLaunchCooperativeKernelMultiDevice(CUDA_LAUNCH_PARAMS* launchParamsList, unsigned int numDevices, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
824 return cydriver._cuLaunchCooperativeKernelMultiDevice(launchParamsList, numDevices, flags)
826cdef CUresult cuLaunchHostFunc(CUstream hStream, CUhostFn fn, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil:
827 return cydriver._cuLaunchHostFunc(hStream, fn, userData)
829cdef CUresult cuLaunchHostFunc_v2(CUstream hStream, CUhostFn fn, void* userData, unsigned int syncMode) except ?CUDA_ERROR_NOT_FOUND nogil:
830 return cydriver._cuLaunchHostFunc_v2(hStream, fn, userData, syncMode)
832cdef CUresult cuFuncSetBlockShape(CUfunction hfunc, int x, int y, int z) except ?CUDA_ERROR_NOT_FOUND nogil:
833 return cydriver._cuFuncSetBlockShape(hfunc, x, y, z)
835cdef CUresult cuFuncSetSharedSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
836 return cydriver._cuFuncSetSharedSize(hfunc, numbytes)
838cdef CUresult cuParamSetSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
839 return cydriver._cuParamSetSize(hfunc, numbytes)
841cdef CUresult cuParamSeti(CUfunction hfunc, int offset, unsigned int value) except ?CUDA_ERROR_NOT_FOUND nogil:
842 return cydriver._cuParamSeti(hfunc, offset, value)
844cdef CUresult cuParamSetf(CUfunction hfunc, int offset, float value) except ?CUDA_ERROR_NOT_FOUND nogil:
845 return cydriver._cuParamSetf(hfunc, offset, value)
847cdef CUresult cuParamSetv(CUfunction hfunc, int offset, void* ptr, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
848 return cydriver._cuParamSetv(hfunc, offset, ptr, numbytes)
850cdef CUresult cuLaunch(CUfunction f) except ?CUDA_ERROR_NOT_FOUND nogil:
851 return cydriver._cuLaunch(f)
853cdef CUresult cuLaunchGrid(CUfunction f, int grid_width, int grid_height) except ?CUDA_ERROR_NOT_FOUND nogil:
854 return cydriver._cuLaunchGrid(f, grid_width, grid_height)
856cdef CUresult cuLaunchGridAsync(CUfunction f, int grid_width, int grid_height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
857 return cydriver._cuLaunchGridAsync(f, grid_width, grid_height, hStream)
859cdef CUresult cuParamSetTexRef(CUfunction hfunc, int texunit, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
860 return cydriver._cuParamSetTexRef(hfunc, texunit, hTexRef)
862cdef CUresult cuFuncSetSharedMemConfig(CUfunction hfunc, CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
863 return cydriver._cuFuncSetSharedMemConfig(hfunc, config)
865cdef CUresult cuGraphCreate(CUgraph* phGraph, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
866 return cydriver._cuGraphCreate(phGraph, flags) 2QxRxSxTxUxVxWxXxYx%kVi'kZxWi(k)k0x1x2x3x4x5x6x7x8xO 9x!x#x$x%x'x(x)x*x+x,x-x.x/x:x;x=x?x@x[x]x^x_x`x{x|x}x~xaybycy*k+k4bXi4d5dYi,k-k.k/k,c6d!g#g$g%g:k;k=k?k5bZi7d8d0i@k[k]k^k-c9d'gSk(g)g_k`k{k1i|kdy2i}k~kal3ibl4icldlelfl6b5i!d#d6iglhliljl.c$d*g+g,g-gklllmlnl7b7i%d'd8iolplqlrl/c(d.g/g:g;gsltlulvl8b9i)d*d!iwlxlylzl:c+d=g?g@g[gAlBlClDl9b#i,d-d$iElFlGlHl;c.d]g^g_g`gIlJlKl%iLl'iMlNlOl(iPl)iQlRlSl*iTl+iUlVl9k0V1V2V3VAw4VDrsrSgpq+c!kIoOoPoQoRolbmbnbob0b1bTb5gWdPiqbrbXdQi8 H , - Ub2bUi[J8g. 9w]J5VTm(b3p/i:i;i=iHyUmVmWmbeceqhIyYmZm1m)b5p[i]i^i_iLy2m3m4mdeeerhMy6m7mzbfege`i+f,f-fadhesh.f/fie1 jebdxcyccdthddedfdAbBbzcuhgdhd] ^ Cb9 ! # $ vh_ ;f=f?f@fwh8m9mAcid[f7p!m#m$m*b8p}i~iajbjNy%m'm(mlemexhOy*m+mcjDb,mzhAhBhChCsdjejfjjdkd]fDshjijjj` ldmdDhneoepeBcqe^fresekjEb.mFhljmjGhEsnjojpjndod_fFsrjsjHhIhteueveweJhxeyezeAe{ pdqdBeCeDerd`fEeFe:m+b#ptjujvjwj;m=m?mGeHeKhTy@m[m{f|f}f~f]m^m_m`m{mLh,bagbgsdtdcgxjIeJeKeLeCcMeyjNeOe-bDcEcFcud.b/b| :b;b=b|m?b$pzjAjBjCjUy}m~manPeQeMhVyOqcnR FbGb@bGcHcIcJc% KcLcvdReSewdTeUeDj[bNhOhVeWePhdndgegfgXexdggfnhgiggn]bEjFjGjHjhninjnYeZeQhknlnRh} Ijkglgmgng(pShThUhMcNc0e)pWhXhmnnn^bzwLjMjNjOjXyonpnqn1e2eYhYysntnHb3e4ePjogpgqgyd5eZhrgsg6e2 7ezdOcPcAd0hBdCdDdIbJbQc1hEdFd~ abKb' ( ) * 2hbbugvgwgxg3hunvnRcGdyg+pwnxnyn_b,pSjTjUjVjZyznAnBn9e!e4h0yDnEnFn`b-pXjYjZj0j2yGnHnIn#e$e5h3yKnLn1jcbHdId6h%e'e(eSc)ezg*e+e2jLbMn8h3j4j9h/J5j6j7jJdKdAgMs9j!j!h#h4g,e-e.e$h/e:e;e=edbLdMd?e@e[eNdBg]e^eNn{b/p#j$j%j'jOnPnQn_e`e%h6yRnSnCgDgEgFgTnUnVnWnXn'h|bGgHgOdPdIg(j{e|e}e~eTcaf)jbfcf}bUcVcWcQd~bacebbcccdcYnec:p*j+j,j-j7yZn0n1ndfef(h8y3n4nS MbNbfcXcYcZc0c+ 1c2cRdffgfSdhfif5ngc.j/jJgKg:j;p)h*h+hjfkf,h=p-h.h7nhc;j=j?j@j8n9n!nlfmfWk#n$n/hfb[jMgNgOgPg@p:h;h=h3c4cnf[p@h[h'n(nOb]pof^j_j`j#y)n*n+npfqf]h$y-n.n/nic{p|j}j~jak'y:n;n=nrfsf^h(y@n[n]njc}pckdkekfk+y^n_n`ntfuf_h,y|n}n~nkcaqhkikjkkk/yaobocovfwf`h:yeofogolccqmknkokpk?yhoiojoxfyf{h@ylomonomceqrksktkuk^yoopoqozfAf|h_ysotouoncgqwkxkykzk{yvowoxoBfCf}h|yzoAoBoochqBkCkDkEk~yCoDoEoDfEf~hazGoHo
868cdef CUresult cuGraphAddKernelNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
869 return cydriver._cuGraphAddKernelNode_v2(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2O hbibjbPbkb4fRk4b,c5b-c6b.c7b/c8b:c9b;c+clbmbnbobTb8 H , - Ub(bbe)bdezbad1 Ab] ^ Cb9 ! # $ _ Ac*bleDbjd` BcEbnd{ +bGe,bLe-bDcEcFcud.b/b| :b;b=b?bPeR % [bXe]bYe} Mc^b1eHbyd2 Ib~ abKb' ( ) * bbRc_b9e`b#ecbScLbJddb{b_e|b~e}bUcVcWcQd~bacebbcccdcecdfS + gcjfhclffb3cObpficrfjctfkcvflcxfmczfncBfocDf
871cdef CUresult cuGraphKernelNodeGetParams(CUgraphNode hNode, CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
872 return cydriver._cuGraphKernelNodeGetParams_v2(hNode, nodeParams) 24f^J!w#wtrlbmbnbobTbH Ub
874cdef CUresult cuGraphKernelNodeSetParams(CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
875 return cydriver._cuGraphKernelNodeSetParams_v2(hNode, nodeParams)
877cdef CUresult cuGraphAddMemcpyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
878 return cydriver._cuGraphAddMemcpyNode(phGraphNode, hGraph, dependencies, numDependencies, copyParams, ctx) 2V W X 6 6d9d$d(d+d.dceeeheBbidmekdqeodrdHeCc| QeR FbGb@bGcHcIcJcwdxdZeNc2e5eJbGd!e$e)eKdNd`eTcebefS MbNbfcXcYcZc0cSdkfmf4cqfsfufwfyfAfCfEf
880cdef CUresult cuGraphMemcpyNodeGetParams(CUgraphNode hNode, CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
881 return cydriver._cuGraphMemcpyNodeGetParams(hNode, nodeParams) 2$w%w'w.
883cdef CUresult cuGraphMemcpyNodeSetParams(CUgraphNode hNode, const CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
884 return cydriver._cuGraphMemcpyNodeSetParams(hNode, nodeParams)
886cdef CUresult cuGraphAddMemsetNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
887 return cydriver._cuGraphAddMemsetNode(phGraphNode, hGraph, dependencies, numDependencies, memsetParams, ctx) 2V W X 6 QbRbSbpc!g#g$g%g'gSk(g)g*g+g,g-g.g/g:g;g=g?g@g[g]g^g_g`gqhrhshzc[fxh]f^f_f`fKhMe:bMh% KcLcvdReSewdTeUeggQh0eYhZhQcyg4h5hzgAgBg%hafbc(h+ 1c2cRdffgfSdhfif,hWknf]h^h_h`h{h|h}h~h
889cdef CUresult cuGraphMemsetNodeGetParams(CUgraphNode hNode, CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
890 return cydriver._cuGraphMemsetNodeGetParams(hNode, nodeParams) 2(w)w*w+w,w-w.w/wurvrwrxr
892cdef CUresult cuGraphMemsetNodeSetParams(CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
893 return cydriver._cuGraphMemsetNodeSetParams(hNode, nodeParams)
895cdef CUresult cuGraphAddHostNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
896 return cydriver._cuGraphAddHostNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2#c$c%c,k-k@k[kglhlolplwlxlElFl0b1b2bUm2m+fddCbwh%mdjnenjIhJhBe;m{f|f}f~fIeud}m@bvddghnShonogBdKb3hznGn%e5j#h$h?eOnCgDgEgFg{eQdZnfcRd)h8n:h)n:n^naohooovoCo
898cdef CUresult cuGraphHostNodeGetParams(CUgraphNode hNode, CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
899 return cydriver._cuGraphHostNodeGetParams(hNode, nodeParams) 2_J`J{J
901cdef CUresult cuGraphHostNodeSetParams(CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
902 return cydriver._cuGraphHostNodeSetParams(hNode, nodeParams)
904cdef CUresult cuGraphAddChildGraphNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
905 return cydriver._cuGraphAddChildGraphNode(phGraphNode, hGraph, dependencies, numDependencies, childGraph) 2N O 4b5b6b7b8b9bTbUb(b)bzb1 ] ^ Cb9 ! # $ _ *bDb` Eb{ +b,b-b?bR % [b]b} ^bHb2 ~ abKb' ( ) * bb_b`bcbLbdb{b|b}becS + gchcfbObicjckclcmcncoc
907cdef CUresult cuGraphChildGraphNodeGetGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
908 return cydriver._cuGraphChildGraphNodeGetGraph(hNode, phGraph) 2O 4b|J5b6b}J7b8b9bTbUb(b)bzb1 ] ^ Cb9 ! # $ _ *bDb` Eb{ +b,b-b?bR % [b]b} ^bHb2 ~ abKb' ( ) * bb_b`bcbLbdb{b|b}becS + gchcfbObicjckclcmcncoc
910cdef CUresult cuGraphAddEmptyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
911 return cydriver._cuGraphAddEmptyNode(phGraphNode, hGraph, dependencies, numDependencies) 2ViWiV W X 6 OkPkQkXi6dZi9d1i2i3i4i5i$d7i(d9i+d#i.d%i'i(i)i*i+isrSg9w]J/ice[ieehebdBb;fid}imezhkdjj` ldmdDhneoepeBcqe^freseFhodrdtjHebgCc| zjQeR FbGb@bGcHcIcJcwdOhxdEjZekgNcLj2e5ezdJbugGdSj!eXj$e1jcbHdId6h%e'e(eSc)ezg*e+e8hKdNd#j`eHgTceb*jefS MbNbfcXcYcZc0cSd/jkf;jmfMg4cofqf|jsfckufhkwfmkyfrkAfwkCfBkEf
913cdef CUresult cuGraphAddEventRecordNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
914 return cydriver._cuGraphAddEventRecordNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2Zb4d7d!d%d)d,d5gWdPiqbrbH :i]ifexc] =f~iAhldljHhIhteuevewepdujsdDcAjFbKcVeFjlgMj3eOc~ vgTjYjHd3j!h#h4g,e-e.eLd$jOdUc+jMb1cJg=jNg^j}jdkiknkskxkCk
916cdef CUresult cuGraphEventRecordNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
917 return cydriver._cuGraphEventRecordNodeGetEvent(hNode, event_out) 2:w;wyr
919cdef CUresult cuGraphEventRecordNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
920 return cydriver._cuGraphEventRecordNodeSetEvent(hNode, event)
922cdef CUresult cuGraphAddEventWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
923 return cydriver._cuGraphAddEventWaitNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2Zb5d8d#d'd*d-dqbrbXdQi;i^igeyc^ ?fajBhmdmjHhJhxeyezeAeqdvjtdEcBjGbLcWeGjmgNj4ePcabwgUjZjId4j!h$h/e:e;e=eMd%jPdVc,jNb2cKg?jOg_j~jekjkoktkykDk
925cdef CUresult cuGraphEventWaitNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
926 return cydriver._cuGraphEventWaitNodeGetEvent(hNode, event_out) 2=w?wzr
928cdef CUresult cuGraphEventWaitNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
929 return cydriver._cuGraphEventWaitNodeSetEvent(hNode, event)
931cdef CUresult cuGraphAddExternalSemaphoresSignalNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
932 return cydriver._cuGraphAddExternalSemaphoresSignalNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
934cdef CUresult cuGraphExternalSemaphoresSignalNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
935 return cydriver._cuGraphExternalSemaphoresSignalNodeGetParams(hNode, params_out)
937cdef CUresult cuGraphExternalSemaphoresSignalNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
938 return cydriver._cuGraphExternalSemaphoresSignalNodeSetParams(hNode, nodeParams)
940cdef CUresult cuGraphAddExternalSemaphoresWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
941 return cydriver._cuGraphAddExternalSemaphoresWaitNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
943cdef CUresult cuGraphExternalSemaphoresWaitNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_WAIT_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
944 return cydriver._cuGraphExternalSemaphoresWaitNodeGetParams(hNode, params_out)
946cdef CUresult cuGraphExternalSemaphoresWaitNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
947 return cydriver._cuGraphExternalSemaphoresWaitNodeSetParams(hNode, nodeParams)
949cdef CUresult cuGraphAddBatchMemOpNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
950 return cydriver._cuGraphAddBatchMemOpNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
952cdef CUresult cuGraphBatchMemOpNodeGetParams(CUgraphNode hNode, CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams_out) except ?CUDA_ERROR_NOT_FOUND nogil:
953 return cydriver._cuGraphBatchMemOpNodeGetParams(hNode, nodeParams_out)
955cdef CUresult cuGraphBatchMemOpNodeSetParams(CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
956 return cydriver._cuGraphBatchMemOpNodeSetParams(hNode, nodeParams)
958cdef CUresult cuGraphExecBatchMemOpNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
959 return cydriver._cuGraphExecBatchMemOpNodeSetParams(hGraphExec, hNode, nodeParams)
961cdef CUresult cuGraphAddMemAllocNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUDA_MEM_ALLOC_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
962 return cydriver._cuGraphAddMemAllocNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2ezfzdiCrAtgzBt%kVi'kWi(k)kNk7c8c9cVdV W X 6 QbRbSbpcmqnqoqOkPkQk*k+kXi4d5dYi,c6d!g#g$g%g=k?kZi7d8d0i-c9d'gSk(g)g{k1i|k2i}k~kal3ibl4icldlelfl5i!d#d6i.c$d*g+g,g-gmlnl7i%d'd8i/c(d.g/g:g;gulvl9i)d*d!i:c+d=g?g@g[gClDl#i,d-d$i;c.d]g^g_g`gKl%iLl'iMlNlOl(iPl)iQlRlSl*iTl+iUlVlSgpqIoWdXd8gTm/i=iceqh1m[i_ieerhzbfege`i+f,f-fadhesh.f/fiebdcdBbzcvh;f@fid[f$m}ibjmexhcjzhChkd]fjj` ldmdDhneoepeBcqe^fresekjFhGhod_f{ pdqdBeCeDerd`fEeFe:mtjwjHeKhLhbgcgCcMeFc| :b|mzjCjQeMhR FbGb@bGcHcIcJc% KcLcvdReSewdTeUeDjOhPhxdgggnEjHjZeQhRhkgngNc0ennLjOj2eYhHb3e4ePjogpgqgyd5eZhrgsg6ezdAdJbQc2hugxgGdygynSjVj!e4hFnXj0j$e5h1jcbHdId6h%e'e(eSc)ezg*e+e2j8h9hKdAgdbLdMd?e@e[eNdBg]e^eNn#j'j`e%h'hHgIgTcafWcebbcYn*j-jef(hS MbNbfcXcYcZc0c+ 1c2cRdffgfSdhfif5n/j:jkf,h7n;j@jmfWk/hMgPg4cnf(nof`jqf]h/n|jaksf^h]nckfkuf_h~nhkkkwf`hgomkpkyf{hnorkukAf|huowkzkCf}hBoBkEkEf~h
964cdef CUresult cuGraphMemAllocNodeGetParams(CUgraphNode hNode, CUDA_MEM_ALLOC_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
965 return cydriver._cuGraphMemAllocNodeGetParams(hNode, params_out) 2di~JaKbKcKNkOkPkQkdKeK:w=w@w!w$w(w)w*w+wfKgKhKiKjKkKlKmKnK;w?w[w#w%w,w-w.w/w]w^w_wyrzrArtrurvrwrxroKpKqKrKsKtKuKvKwKxKyKzKAKSgof
967cdef CUresult cuGraphAddMemFreeNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
968 return cydriver._cuGraphAddMemFreeNode(phGraphNode, hGraph, dependencies, numDependencies, dptr) 2diNk7c8c9cVdV W X 6 QbRbSbpcYi0i6i8i!i$iDr8g=i_i`icd@fbjChDhGh{ pdqdBeCeDerd`fEeFewjcgFcCjPhHjngOjPjAdxgVj0j6h9hdbLdMd?e@e[eNdBg]e^e'jIgWc-j:j@jPg`jakfkkkpkukzkEk
970cdef CUresult cuGraphMemFreeNodeGetParams(CUgraphNode hNode, CUdeviceptr* dptr_out) except ?CUDA_ERROR_NOT_FOUND nogil:
971 return cydriver._cuGraphMemFreeNodeGetParams(hNode, dptr_out) 2di@w[wAr
973cdef CUresult cuDeviceGraphMemTrim(CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
974 return cydriver._cuDeviceGraphMemTrim(device) 1YZ0
976cdef CUresult cuDeviceGetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
977 return cydriver._cuDeviceGetGraphMemAttribute(device, attr, value) 2Y Z 0 8g
979cdef CUresult cuDeviceSetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
980 return cydriver._cuDeviceSetGraphMemAttribute(device, attr, value) 1YZ0
982cdef CUresult cuGraphClone(CUgraph* phGraphClone, CUgraph originalGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
983 return cydriver._cuGraphClone(phGraphClone, originalGraph) 2qb,
985cdef CUresult cuGraphNodeFindInClone(CUgraphNode* phNode, CUgraphNode hOriginalNode, CUgraph hClonedGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
986 return cydriver._cuGraphNodeFindInClone(phNode, hOriginalNode, hClonedGraph)
988cdef CUresult cuGraphNodeGetType(CUgraphNode hNode, CUgraphNodeType* typename) except ?CUDA_ERROR_NOT_FOUND nogil:
989 return cydriver._cuGraphNodeGetType(hNode, typename) 2di6q~JaKbKcKNkOkPkQk4f^JdKeK|J:w=w@w_J!w$w(w)w*w+wfKgKhKiKjKkKlKmK}JnK;w?w[w`J{J6V7V#w%w,w-w.w/w8V9V]w^w_wyrzrArtr'wurvrwrxr!Z#Z$Z%Z'Z(Z)Z*Z+Z,Z-Z.Z/Z:Z;Z=Z?Z@Z[ZoKpKqKrKsKtKuKvKwKxKyKzK!VAKsrSglbmbnbobTbH UbUiof
991cdef CUresult cuGraphNodeGetContainingGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
992 return cydriver._cuGraphNodeGetContainingGraph(hNode, phGraph)
994cdef CUresult cuGraphNodeGetLocalId(CUgraphNode hNode, unsigned int* nodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
995 return cydriver._cuGraphNodeGetLocalId(hNode, nodeId)
997cdef CUresult cuGraphNodeGetToolsId(CUgraphNode hNode, unsigned long long* toolsNodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
998 return cydriver._cuGraphNodeGetToolsId(hNode, toolsNodeId)
1000cdef CUresult cuGraphGetId(CUgraph hGraph, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1001 return cydriver._cuGraphGetId(hGraph, graphId)
1003cdef CUresult cuGraphExecGetId(CUgraphExec hGraphExec, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1004 return cydriver._cuGraphExecGetId(hGraphExec, graphId)
1006cdef CUresult cuGraphGetNodes(CUgraph hGraph, CUgraphNode* nodes, size_t* numNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1007 return cydriver._cuGraphGetNodes(hGraph, nodes, numNodes) 26q^JdKeK|J:w=w@w_J!w$w(w)w*w+wfKgKhK]ZiKjKkKlKmK}JnK;w?w[w`J{J6V7V#w%w,w-w.w/w8V9VoKpKqKrKsKtKsrOoPoQoRolbmbnbobTbUbUiOb
1009cdef CUresult cuGraphGetRootNodes(CUgraph hGraph, CUgraphNode* rootNodes, size_t* numRootNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1010 return cydriver._cuGraphGetRootNodes(hGraph, rootNodes, numRootNodes)
1012cdef CUresult cuGraphGetEdges(CUgraph hGraph, CUgraphNode* from_, CUgraphNode* to, CUgraphEdgeData* edgeData, size_t* numEdges) except ?CUDA_ERROR_NOT_FOUND nogil:
1013 return cydriver._cuGraphGetEdges_v2(hGraph, from_, to, edgeData, numEdges) 2~JaK^Z_ZbKcK`Z
1015cdef CUresult cuGraphNodeGetDependencies(CUgraphNode hNode, CUgraphNode* dependencies, CUgraphEdgeData* edgeData, size_t* numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1016 return cydriver._cuGraphNodeGetDependencies_v2(hNode, dependencies, edgeData, numDependencies) 2diNkOkPkQk4f]w^w{Z_wyrzrAr|Z}Z~Za0tr'wurvrwrxrb0c0uKvKd0wKxKe0SgH of
1018cdef CUresult cuGraphNodeGetDependentNodes(CUgraphNode hNode, CUgraphNode* dependentNodes, CUgraphEdgeData* edgeData, size_t* numDependentNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1019 return cydriver._cuGraphNodeGetDependentNodes_v2(hNode, dependentNodes, edgeData, numDependentNodes) 2]w^w_wyrzrArtr'wurvrwrxryKzKf0!VAKg0
1021cdef CUresult cuGraphAddDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1022 return cydriver._cuGraphAddDependencies_v2(hGraph, from_, to, edgeData, numDependencies)
1024cdef CUresult cuGraphRemoveDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1025 return cydriver._cuGraphRemoveDependencies_v2(hGraph, from_, to, edgeData, numDependencies)
1027cdef CUresult cuGraphDestroyNode(CUgraphNode hNode) except ?CUDA_ERROR_NOT_FOUND nogil:
1028 return cydriver._cuGraphDestroyNode(hNode) 2]J
1030cdef CUresult cuGraphInstantiate(CUgraphExec* phGraphExec, CUgraph hGraph, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1031 return cydriver._cuGraphInstantiateWithFlags(phGraphExec, hGraph, flags) 2qb, 8g. 9w
1033cdef CUresult cuGraphInstantiateWithParams(CUgraphExec* phGraphExec, CUgraph hGraph, CUDA_GRAPH_INSTANTIATE_PARAMS* instantiateParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1034 return cydriver._cuGraphInstantiateWithParams(phGraphExec, hGraph, instantiateParams) 2N gbB *cM T U 4 WbXbYb'c(c)cv w x y z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G #c7c8c9cVdO Zb$c%chbibjbPbkbV W X 6 QbRbSbpc#V$V%Vmqnqoq+cIo0b1brbH - 2bVb
1036cdef CUresult cuGraphExecGetFlags(CUgraphExec hGraphExec, cuuint64_t* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1037 return cydriver._cuGraphExecGetFlags(hGraphExec, flags)
1039cdef CUresult cuGraphExecKernelNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1040 return cydriver._cuGraphExecKernelNodeSetParams_v2(hGraphExec, hNode, nodeParams)
1042cdef CUresult cuGraphExecMemcpyNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1043 return cydriver._cuGraphExecMemcpyNodeSetParams(hGraphExec, hNode, copyParams, ctx)
1045cdef CUresult cuGraphExecMemsetNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1046 return cydriver._cuGraphExecMemsetNodeSetParams(hGraphExec, hNode, memsetParams, ctx)
1048cdef CUresult cuGraphExecHostNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1049 return cydriver._cuGraphExecHostNodeSetParams(hGraphExec, hNode, nodeParams)
1051cdef CUresult cuGraphExecChildGraphNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1052 return cydriver._cuGraphExecChildGraphNodeSetParams(hGraphExec, hNode, childGraph)
1054cdef CUresult cuGraphExecEventRecordNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1055 return cydriver._cuGraphExecEventRecordNodeSetEvent(hGraphExec, hNode, event)
1057cdef CUresult cuGraphExecEventWaitNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1058 return cydriver._cuGraphExecEventWaitNodeSetEvent(hGraphExec, hNode, event)
1060cdef CUresult cuGraphExecExternalSemaphoresSignalNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1061 return cydriver._cuGraphExecExternalSemaphoresSignalNodeSetParams(hGraphExec, hNode, nodeParams)
1063cdef CUresult cuGraphExecExternalSemaphoresWaitNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1064 return cydriver._cuGraphExecExternalSemaphoresWaitNodeSetParams(hGraphExec, hNode, nodeParams)
1066cdef CUresult cuGraphNodeSetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1067 return cydriver._cuGraphNodeSetEnabled(hGraphExec, hNode, isEnabled)
1069cdef CUresult cuGraphNodeGetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int* isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1070 return cydriver._cuGraphNodeGetEnabled(hGraphExec, hNode, isEnabled)
1072cdef CUresult cuGraphUpload(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1073 return cydriver._cuGraphUpload(hGraphExec, hStream) 2M 4 v w x y z A J K L sbtbubY Z 0 #c7c8c9cO Zb$c%chbibjbkbV W X QbRbSb0b1b2b
1075cdef CUresult cuGraphLaunch(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1076 return cydriver._cuGraphLaunch(hGraphExec, hStream) 2N B M U 4 v w x y z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G #c7c8c9cVdO Zb$c%chbibjbPbkbV W X 6 QbRbSbpc0b1bqbrbH , - 2b8g.
1078cdef CUresult cuGraphExecDestroy(CUgraphExec hGraphExec) except ?CUDA_ERROR_NOT_FOUND nogil:
1079 return cydriver._cuGraphExecDestroy(hGraphExec) 2N gbB *cM T U 4 WbXbYb'c(c)cv w x y z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G #c7c8c9cVdO Zb$c%chbibjbPbkbV W X 6 QbRbSbpc#V$V%Vmqnqoq0b1brbH - 2bVb'V. 9w
1081cdef CUresult cuGraphDestroy(CUgraph hGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1082 return cydriver._cuGraphDestroy(hGraph) 2N gbB *cM OiT U 4 WbXbYb'c(c)cv w x y z A J K L sbtbubY Z 0 b c d e f g h i j k l m n o p q r s t u D E F G {A|A}A~AaBbBcBdBeBfBgBhBiBjBkBlBmBnBoBpBqBrBsBtBuBO vBXtwBxByBzBABBBCBDBEBFBGBHBIBJBKBLBMBNBOBPBQBRBSBTBUBVBWBXB4bYBYtZtZB0B1B2B3B4B5B6B7B8B9B!B#B$B5b%B0t1t'B(B)B*B+B,B-B.B/B:B;B=B?B@B[B]B^B_B`B{B|B}B~B6baCbC2t3tcCdCeCfCgChCiCjCkClCmCnCoCpCqC7brCsC4t5ttCuCvCwCxCyCzCACBCCCDCECFCGCHC8bICJC6t7tKCLCMCNCOCPCQCRCSCTCUCVCWCXCYC9bZC0C8t9t1C2C3C4C5C6C7C8C9C!C#C$C%C'C(C)C*C+C,C-C.C/C:C;C=C?C@C[C]C^C_C9k0V1V2V3VAw4VDrsrSgpq!kOoPoQoRolbmbnbob0b1bTb5gWdPiqbrbXdQi8 H , - Ub2b3dVbI 'V8g. 5V`C(b|C}C~C!t#tbDcDdDeDfDgDhDiDjDlDmDpD)brDsDtD$t%tvDwDxDyDzDADBDCDDDFDGDzbHD't(tIDJDKDLDMDNDODPDQD)t1 *t+t,tGqHq-t.t/t:t;t=t?t@t[t]t^t] _t^ `tCbUD9 VD! WD# XD$ YDZD_ 0D1D{t|t2D3D4D5D6D7D8D9D!D#D$D*b'D(D)D}t~t*D+D,D-D.D/D:D;D=D?D@D[DDb^D_D`Daubu|D}D~DaEbEcEdEeEfEhEiEjE` kEcudulEmEnEoEpEqErEsEtEeuEbguhuiujukulumunuoupuqurusutuuuvuwuxuyuzuAuBuCuDuEuFuGu{ yEHuIuzEAEBECEDEEEFEGE+bHEIEJEJuKuKELEMENEOEPEQERESETEUEVEWEXEYEZE0E1E2E3E,b4E5E6ELuMu7E8E9E!E#E$E%E'E(E)E*E-b+ENuOu,E-E.E/E:E;E=E?E@E?b[E]E^EPuQu_E`E{E|E}E~EaFbFcFdFeFR fFRuSugFhFiFjFkF% lFTuUumFnFoFpFqFrFsF[btFuFvFVuWuwFxFyFzFAFBFCFDFEFFFGFHF]bIFJFXuYuKFLFMFNFOFPFQFRFSFZu} 1u2u3uIqJq5u6u7u8u9u!u#u$u%u'u(uXFYF^b0F1F2F)u*u4F5F6F7F8F9F!F#F$F'F(FHb)F+u,u*F+F,F-F.F/F:F;F=F-u2 .u/u:uKqLq;u=u?u@u[u]u^u_u`u{u|u~ }uab~uKb]F' ^F( _F) `F* {F|Fbb}F~FavbvaGbGcGdGeGfGgGhGiGjGkG_bmGnGoGcvdvpGqGrGsGtGuGvGwGxGyGzGAG`bCGDGEGevfvGGHGIGJGKGLGMGNGOGQGRGSGcbTGgvhvUGVGWGXGYGZG0G1G2GivLbkvlvmvnvovpvqvrvsvtvuvvvwvxvyvzvAvBvCvDvEvFvGvHvIvJvKvdb7GLvMv8G9G!G#G$G%G'G(G{b)G*G+GNvOv,G-G.G/G:G;G=G?G@G[G]G^G_G`G{G|G}G~GaHbH|bcHdHeHPvQvfHgHhHiHjHkHlHmHnHoHpH}bqHRvSvrHsHtHuHvHwHxHyHzHecAHBHCHTvUvDHEHFHGHHHIHJHKHLHMHNHS OHVvWvPHQHRHSHTH+ UHXvYvVHWHXHYHZH0H1Hgc2H3H4HZv0v5H6H7H8H9H!H#H$H%H'H(H)Hhc*H+H1v2v,H-H.H/H:H;H=H?H@H3vfb5v6v7vMqNq9v!v#v$v%v'v(v)v*v+v,v`H{HOb}H~HaI-v.vcIdIeIfIgIhIiIjIkImInIoIicqIrIsI/v:vuIvIwIxIyIzIAIBICIEIFIGIjcIIJIKI;v=vMINIOIPIQIRISITIUIWIXIYIkc0I1I2I?v@v4I5I6I7I8I9I!I#I$I'I(I)Ilc+I,I-I[v]v/I:I;I=I?I@I[I]I^I`I{I|Imc~IaJbJ^v_vdJeJfJgJhJiJjJkJlJnJoJpJncrJsJtJ`v{vvJwJxJyJzJAJBJCJDJFJGJHJocJJKJLJ|v}vNJOJPJQJRJSJTJUJVJXJYJ
1084cdef CUresult cuGraphExecUpdate(CUgraphExec hGraphExec, CUgraph hGraph, CUgraphExecUpdateResultInfo* resultInfo) except ?CUDA_ERROR_NOT_FOUND nogil:
1085 return cydriver._cuGraphExecUpdate_v2(hGraphExec, hGraph, resultInfo) 1B
1087cdef CUresult cuGraphKernelNodeCopyAttributes(CUgraphNode dst, CUgraphNode src) except ?CUDA_ERROR_NOT_FOUND nogil:
1088 return cydriver._cuGraphKernelNodeCopyAttributes(dst, src)
1090cdef CUresult cuGraphKernelNodeGetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, CUkernelNodeAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1091 return cydriver._cuGraphKernelNodeGetAttribute(hNode, attr, value_out)
1093cdef CUresult cuGraphKernelNodeSetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, const CUkernelNodeAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1094 return cydriver._cuGraphKernelNodeSetAttribute(hNode, attr, value)
1096cdef CUresult cuGraphDebugDotPrint(CUgraph hGraph, const char* path, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1097 return cydriver._cuGraphDebugDotPrint(hGraph, path, flags) 2AtBtI
1099cdef CUresult cuUserObjectCreate(CUuserObject* object_out, void* ptr, CUhostFn destroy, unsigned int initialRefcount, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1100 return cydriver._cuUserObjectCreate(object_out, ptr, destroy, initialRefcount, flags) 2#cO Zb$c%chbibjbPbkb4fRk4b4d5d,k-k,c5b7d8d@k[k-c6b!d#dglhl.c7b%d'dolpl/c8b)d*dwlxl:c9b,d-dElFl;c+clbmbnbob0b1bTb5gWdPiqbrbXdQi8 H , - Ub2b(b:i;iUmbe)b]i^i2mdezbfege+fad1 xcycddAb] ^ Cb9 ! # $ _ =f?fwhAc*b~iaj%mleDbAhBhdjjd` ldmdneBcEbljmjnjndHhIhteueveweJhxeyezeAe{ pdqdBe+bujvj;mGe{f|f}f~f,bsdtdIeLe-bDcEcFcud.b/b| :b;b=b?bAjBj}mPeR FbGb@b% KcLcvd[bVeWedgXe]bFjGjhnYe} lgmgShMc^bMjNjon1eHb3e4eogyd2 OcPcBdIb~ abKb' ( ) * bbvgwg3hRc_bTjUjzn9e`bYjZjGn#ecbHdId%eScLb3j4j5jJd!h#h4g,e-e.e$h/e:e;e=edbLdMd?e{b$j%jOn_eCgDgEgFg|bOdPd{e~e}bUcVcWcQd~bacebbcccdcec+j,jZndfS MbNbfc+ 1c2cRdgcJgKg)hjfhc=j?j8nlffbNgOg:h3cOb^j_j)npfic}j~j:nrfjcdkek^ntfkcikjkaovflcnkokhoxfmcsktkoozfncxkykvoBfocCkDkCoDf
1102cdef CUresult cuUserObjectRetain(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1103 return cydriver._cuUserObjectRetain(object, count)
1105cdef CUresult cuUserObjectRelease(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1106 return cydriver._cuUserObjectRelease(object, count)
1108cdef CUresult cuGraphRetainUserObject(CUgraph graph, CUuserObject object, unsigned int count, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1109 return cydriver._cuGraphRetainUserObject(graph, object, count, flags) 2#cO Zb$c%chbibjbPbkb4fRk4b4d5d,k-k,c5b7d8d@k[k-c6b!d#dglhl.c7b%d'dolpl/c8b)d*dwlxl:c9b,d-dElFl;c+clbmbnbob0b1bTb5gWdPiqbrbXdQi8 H , - Ub2b(b:i;iUmbe)b]i^i2mdezbfege+fad1 xcycddAb] ^ Cb9 ! # $ _ =f?fwhAc*b~iaj%mleDbAhBhdjjd` ldmdneBcEbljmjnjndHhIhteueveweJhxeyezeAe{ pdqdBe+bujvj;mGe{f|f}f~f,bsdtdIeLe-bDcEcFcud.b/b| :b;b=b?bAjBj}mPeR FbGb@b% KcLcvd[bVeWedgXe]bFjGjhnYe} lgmgShMc^bMjNjon1eHb3e4eogyd2 OcPcBdIb~ abKb' ( ) * bbvgwg3hRc_bTjUjzn9e`bYjZjGn#ecbHdId%eScLb3j4j5jJd!h#h4g,e-e.e$h/e:e;e=edbLdMd?e{b$j%jOn_eCgDgEgFg|bOdPd{e~e}bUcVcWcQd~bacebbcccdcec+j,jZndfS MbNbfc+ 1c2cRdgcJgKg)hjfhc=j?j8nlffbNgOg:h3cOb^j_j)npfic}j~j:nrfjcdkek^ntfkcikjkaovflcnkokhoxfmcsktkoozfncxkykvoBfocCkDkCoDf
1111cdef CUresult cuGraphReleaseUserObject(CUgraph graph, CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1112 return cydriver._cuGraphReleaseUserObject(graph, object, count)
1114cdef CUresult cuGraphAddNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1115 return cydriver._cuGraphAddNode_v2(phGraphNode, hGraph, dependencies, dependencyData, numDependencies, nodeParams) 2B b c d e f g h i j k l m n o p q r s t u D E F G 6q.k/k:k;k]k^k_k`kiljlklllqlrlsltlylzlAlBlGlHlIlJl9k!kOoPoQoRolbmbnbobUiI [J. VmWmYmZm3m4m6m7m,f-f.f/fedfdgdhd9 ! # $ 8m9m!m#m'm(m*m+mejfjhjijoepereseojpjrjsjteuevewexeyezeAeCeDeEeFe=m?m@m[m{f|f}f~f]m^m_m`m{mJeKeNeOe.b/b;b=b~manOqcnGcHcIcJcReSeTeUeegfghgiginjnknlnThUhWhXhmnpnqnsntnpgqgrgsgCdDdEdFd' ( ) * unvnwnxnAnBnDnEnHnInKnLn'e(e*e+e6j7j9j!j4g,e-e.e/e:e;e=e@e[e]e^ePnQnRnSnCgDgEgFgTnUnVnWnXn|e}ebfcf~bacccdc0n1n3n4nXcYcZc0cffgfhfif*h+h-h.h9n!n#n$n;h=h@h[h'n*n+n-n.n;n=n@n[n_n`n|n}nbocoeofoiojolomopoqosotowoxozoAoDoEoGoHo
1117cdef CUresult cuGraphNodeSetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1118 return cydriver._cuGraphNodeSetParams(hNode, nodeParams) 1.
1120cdef CUresult cuGraphNodeGetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1121 return cydriver._cuGraphNodeGetParams(hNode, nodeParams)
1123cdef CUresult cuGraphExecNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1124 return cydriver._cuGraphExecNodeSetParams(hGraphExec, hNode, nodeParams) 1.
1126cdef CUresult cuGraphConditionalHandleCreate(CUgraphConditionalHandle* pHandle_out, CUgraph hGraph, CUcontext ctx, unsigned int defaultLaunchValue, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1127 return cydriver._cuGraphConditionalHandleCreate(pHandle_out, hGraph, ctx, defaultLaunchValue, flags) 2B b c d e f g h i j k l m n o p q r s t u D E F G 6q.k/k:k;k]k^k_k`kiljlklllqlrlsltlylzlAlBlGlHlIlJl9kAw!kOoPoQoRolbmbnbobUiI [J3pVmWmYmZm5p3m4m6m7m,f-f.f/fjeedfdgdhd9 ! # $ vh_ ;f=f?f@fwh8m9mAcid[f7p!m#m8p'm(m*m+m,mejfjhjijoeperese.mojpjrjsjteuevewexeyezeAeCeDeEeFe#p=m?m@m[m{f|f}f~f]m^m_m`m{magJeKeNeOe.b/b;b=b$p~manOqcnGcHcIcJcReSeTeUeNhegfghgiginjnknlnIjThUhWhXhmnzwpnqnsntnpgqgrgsg7eCdDdEdFd' ( ) * 2hbbugvgwgxg3hunvnRcGdyg+pwnxn,pAnBnDnEn-pHnInKnLn'e(e*e+eMn6j7j9j!j4g,e-e.e/e:e;e=e@e[e]e^e/pPnQnRnSnCgDgEgFgTnUnVnWnXnGg|e}ebfcf~bacccdc:p0n1n3n4nXcYcZc0cffgfhfif.j*h+h-h.h9n!n#n$n[j;h=h@h[h'n]p*n+n-n.n{p;n=n@n[n}p_n`n|n}naqbocoeofocqiojolomoeqpoqosotogqwoxozoAohqDoEoGoHo
1129cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize) except ?CUDA_ERROR_NOT_FOUND nogil:
1130 return cydriver._cuOccupancyMaxActiveBlocksPerMultiprocessor(numBlocks, func, blockSize, dynamicSMemSize) 20dFtGtHtItJtKtLtMtNtOtPtQtRtStTtUtVtWt
1132cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1133 return cydriver._cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(numBlocks, func, blockSize, dynamicSMemSize, flags)
1135cdef CUresult cuOccupancyMaxPotentialBlockSize(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit) except ?CUDA_ERROR_NOT_FOUND nogil:
1136 return cydriver._cuOccupancyMaxPotentialBlockSize(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit) 2#A$A%A'A(A)A*A+A,A-A.A/A:A;A=A?A@A[A]A^A_A
1138cdef CUresult cuOccupancyMaxPotentialBlockSizeWithFlags(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1139 return cydriver._cuOccupancyMaxPotentialBlockSizeWithFlags(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit, flags)
1141cdef CUresult cuOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, CUfunction func, int numBlocks, int blockSize) except ?CUDA_ERROR_NOT_FOUND nogil:
1142 return cydriver._cuOccupancyAvailableDynamicSMemPerBlock(dynamicSmemSize, func, numBlocks, blockSize) 25A6A7A8A9A!A
1144cdef CUresult cuOccupancyMaxPotentialClusterSize(int* clusterSize, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1145 return cydriver._cuOccupancyMaxPotentialClusterSize(clusterSize, func, config)
1147cdef CUresult cuOccupancyMaxActiveClusters(int* numClusters, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1148 return cydriver._cuOccupancyMaxActiveClusters(numClusters, func, config)
1150cdef CUresult cuTexRefSetArray(CUtexref hTexRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1151 return cydriver._cuTexRefSetArray(hTexRef, hArray, Flags)
1153cdef CUresult cuTexRefSetMipmappedArray(CUtexref hTexRef, CUmipmappedArray hMipmappedArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1154 return cydriver._cuTexRefSetMipmappedArray(hTexRef, hMipmappedArray, Flags)
1156cdef CUresult cuTexRefSetAddress(size_t* ByteOffset, CUtexref hTexRef, CUdeviceptr dptr, size_t numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1157 return cydriver._cuTexRefSetAddress_v2(ByteOffset, hTexRef, dptr, numbytes)
1159cdef CUresult cuTexRefSetAddress2D(CUtexref hTexRef, const CUDA_ARRAY_DESCRIPTOR* desc, CUdeviceptr dptr, size_t Pitch) except ?CUDA_ERROR_NOT_FOUND nogil:
1160 return cydriver._cuTexRefSetAddress2D_v3(hTexRef, desc, dptr, Pitch)
1162cdef CUresult cuTexRefSetFormat(CUtexref hTexRef, CUarray_format fmt, int NumPackedComponents) except ?CUDA_ERROR_NOT_FOUND nogil:
1163 return cydriver._cuTexRefSetFormat(hTexRef, fmt, NumPackedComponents)
1165cdef CUresult cuTexRefSetAddressMode(CUtexref hTexRef, int dim, CUaddress_mode am) except ?CUDA_ERROR_NOT_FOUND nogil:
1166 return cydriver._cuTexRefSetAddressMode(hTexRef, dim, am)
1168cdef CUresult cuTexRefSetFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1169 return cydriver._cuTexRefSetFilterMode(hTexRef, fm)
1171cdef CUresult cuTexRefSetMipmapFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1172 return cydriver._cuTexRefSetMipmapFilterMode(hTexRef, fm)
1174cdef CUresult cuTexRefSetMipmapLevelBias(CUtexref hTexRef, float bias) except ?CUDA_ERROR_NOT_FOUND nogil:
1175 return cydriver._cuTexRefSetMipmapLevelBias(hTexRef, bias)
1177cdef CUresult cuTexRefSetMipmapLevelClamp(CUtexref hTexRef, float minMipmapLevelClamp, float maxMipmapLevelClamp) except ?CUDA_ERROR_NOT_FOUND nogil:
1178 return cydriver._cuTexRefSetMipmapLevelClamp(hTexRef, minMipmapLevelClamp, maxMipmapLevelClamp)
1180cdef CUresult cuTexRefSetMaxAnisotropy(CUtexref hTexRef, unsigned int maxAniso) except ?CUDA_ERROR_NOT_FOUND nogil:
1181 return cydriver._cuTexRefSetMaxAnisotropy(hTexRef, maxAniso)
1183cdef CUresult cuTexRefSetBorderColor(CUtexref hTexRef, float* pBorderColor) except ?CUDA_ERROR_NOT_FOUND nogil:
1184 return cydriver._cuTexRefSetBorderColor(hTexRef, pBorderColor)
1186cdef CUresult cuTexRefSetFlags(CUtexref hTexRef, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1187 return cydriver._cuTexRefSetFlags(hTexRef, Flags)
1189cdef CUresult cuTexRefGetAddress(CUdeviceptr* pdptr, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1190 return cydriver._cuTexRefGetAddress_v2(pdptr, hTexRef)
1192cdef CUresult cuTexRefGetArray(CUarray* phArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1193 return cydriver._cuTexRefGetArray(phArray, hTexRef)
1195cdef CUresult cuTexRefGetMipmappedArray(CUmipmappedArray* phMipmappedArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1196 return cydriver._cuTexRefGetMipmappedArray(phMipmappedArray, hTexRef)
1198cdef CUresult cuTexRefGetAddressMode(CUaddress_mode* pam, CUtexref hTexRef, int dim) except ?CUDA_ERROR_NOT_FOUND nogil:
1199 return cydriver._cuTexRefGetAddressMode(pam, hTexRef, dim)
1201cdef CUresult cuTexRefGetFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1202 return cydriver._cuTexRefGetFilterMode(pfm, hTexRef)
1204cdef CUresult cuTexRefGetFormat(CUarray_format* pFormat, int* pNumChannels, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1205 return cydriver._cuTexRefGetFormat(pFormat, pNumChannels, hTexRef)
1207cdef CUresult cuTexRefGetMipmapFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1208 return cydriver._cuTexRefGetMipmapFilterMode(pfm, hTexRef)
1210cdef CUresult cuTexRefGetMipmapLevelBias(float* pbias, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1211 return cydriver._cuTexRefGetMipmapLevelBias(pbias, hTexRef)
1213cdef CUresult cuTexRefGetMipmapLevelClamp(float* pminMipmapLevelClamp, float* pmaxMipmapLevelClamp, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1214 return cydriver._cuTexRefGetMipmapLevelClamp(pminMipmapLevelClamp, pmaxMipmapLevelClamp, hTexRef)
1216cdef CUresult cuTexRefGetMaxAnisotropy(int* pmaxAniso, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1217 return cydriver._cuTexRefGetMaxAnisotropy(pmaxAniso, hTexRef)
1219cdef CUresult cuTexRefGetBorderColor(float* pBorderColor, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1220 return cydriver._cuTexRefGetBorderColor(pBorderColor, hTexRef)
1222cdef CUresult cuTexRefGetFlags(unsigned int* pFlags, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1223 return cydriver._cuTexRefGetFlags(pFlags, hTexRef)
1225cdef CUresult cuTexRefCreate(CUtexref* pTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1226 return cydriver._cuTexRefCreate(pTexRef)
1228cdef CUresult cuTexRefDestroy(CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1229 return cydriver._cuTexRefDestroy(hTexRef)
1231cdef CUresult cuSurfRefSetArray(CUsurfref hSurfRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1232 return cydriver._cuSurfRefSetArray(hSurfRef, hArray, Flags)
1234cdef CUresult cuSurfRefGetArray(CUarray* phArray, CUsurfref hSurfRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1235 return cydriver._cuSurfRefGetArray(phArray, hSurfRef)
1237cdef CUresult cuTexObjectCreate(CUtexObject* pTexObject, const CUDA_RESOURCE_DESC* pResDesc, const CUDA_TEXTURE_DESC* pTexDesc, const CUDA_RESOURCE_VIEW_DESC* pResViewDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
1238 return cydriver._cuTexObjectCreate(pTexObject, pResDesc, pTexDesc, pResViewDesc)
1240cdef CUresult cuTexObjectDestroy(CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1241 return cydriver._cuTexObjectDestroy(texObject)
1243cdef CUresult cuTexObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1244 return cydriver._cuTexObjectGetResourceDesc(pResDesc, texObject)
1246cdef CUresult cuTexObjectGetTextureDesc(CUDA_TEXTURE_DESC* pTexDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1247 return cydriver._cuTexObjectGetTextureDesc(pTexDesc, texObject)
1249cdef CUresult cuTexObjectGetResourceViewDesc(CUDA_RESOURCE_VIEW_DESC* pResViewDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1250 return cydriver._cuTexObjectGetResourceViewDesc(pResViewDesc, texObject)
1252cdef CUresult cuSurfObjectCreate(CUsurfObject* pSurfObject, const CUDA_RESOURCE_DESC* pResDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
1253 return cydriver._cuSurfObjectCreate(pSurfObject, pResDesc)
1255cdef CUresult cuSurfObjectDestroy(CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1256 return cydriver._cuSurfObjectDestroy(surfObject)
1258cdef CUresult cuSurfObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1259 return cydriver._cuSurfObjectGetResourceDesc(pResDesc, surfObject)
1261cdef CUresult cuTensorMapEncodeTiled(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, const cuuint32_t* boxDim, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil:
1262 return cydriver._cuTensorMapEncodeTiled(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, boxDim, elementStrides, interleave, swizzle, l2Promotion, oobFill)
1264cdef CUresult cuTensorMapEncodeIm2col(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, const int* pixelBoxLowerCorner, const int* pixelBoxUpperCorner, cuuint32_t channelsPerPixel, cuuint32_t pixelsPerColumn, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil:
1265 return cydriver._cuTensorMapEncodeIm2col(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCorner, pixelBoxUpperCorner, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, swizzle, l2Promotion, oobFill)
1267cdef CUresult cuTensorMapEncodeIm2colWide(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, int pixelBoxLowerCornerWidth, int pixelBoxUpperCornerWidth, cuuint32_t channelsPerPixel, cuuint32_t pixelsPerColumn, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapIm2ColWideMode mode, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil:
1268 return cydriver._cuTensorMapEncodeIm2colWide(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCornerWidth, pixelBoxUpperCornerWidth, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, mode, swizzle, l2Promotion, oobFill)
1270cdef CUresult cuTensorMapReplaceAddress(CUtensorMap* tensorMap, void* globalAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1271 return cydriver._cuTensorMapReplaceAddress(tensorMap, globalAddress)
1273cdef CUresult cuDeviceCanAccessPeer(int* canAccessPeer, CUdevice dev, CUdevice peerDev) except ?CUDA_ERROR_NOT_FOUND nogil:
1274 return cydriver._cuDeviceCanAccessPeer(canAccessPeer, dev, peerDev)
1276cdef CUresult cuCtxEnablePeerAccess(CUcontext peerContext, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1277 return cydriver._cuCtxEnablePeerAccess(peerContext, Flags)
1279cdef CUresult cuCtxDisablePeerAccess(CUcontext peerContext) except ?CUDA_ERROR_NOT_FOUND nogil:
1280 return cydriver._cuCtxDisablePeerAccess(peerContext)
1282cdef CUresult cuDeviceGetP2PAttribute(int* value, CUdevice_P2PAttribute attrib, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil:
1283 return cydriver._cuDeviceGetP2PAttribute(value, attrib, srcDevice, dstDevice)
1285cdef CUresult cuDeviceGetP2PAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil:
1286 return cydriver._cuDeviceGetP2PAtomicCapabilities(capabilities, operations, count, srcDevice, dstDevice)
1288cdef CUresult cuGraphicsUnregisterResource(CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1289 return cydriver._cuGraphicsUnregisterResource(resource) 2VgWgXgMo(V)V*V+V,V-VYgZg0gni1gBr2g.V3g7f/V:V;VNo
1291cdef CUresult cuGraphicsSubResourceGetMappedArray(CUarray* pArray, CUgraphicsResource resource, unsigned int arrayIndex, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil:
1292 return cydriver._cuGraphicsSubResourceGetMappedArray(pArray, resource, arrayIndex, mipLevel)
1294cdef CUresult cuGraphicsResourceGetMappedMipmappedArray(CUmipmappedArray* pMipmappedArray, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1295 return cydriver._cuGraphicsResourceGetMappedMipmappedArray(pMipmappedArray, resource)
1297cdef CUresult cuGraphicsResourceGetMappedPointer(CUdeviceptr* pDevPtr, size_t* pSize, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1298 return cydriver._cuGraphicsResourceGetMappedPointer_v2(pDevPtr, pSize, resource) 2VgLoWgXgYgZg0gni1gBr2g3gXk
1300cdef CUresult cuGraphicsResourceSetMapFlags(CUgraphicsResource resource, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1301 return cydriver._cuGraphicsResourceSetMapFlags_v2(resource, flags)
1303cdef CUresult cuGraphicsMapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1304 return cydriver._cuGraphicsMapResources(count, resources, hStream) 2VgLoWgXgYgZg0gni1gBr2g3gXk
1306cdef CUresult cuGraphicsUnmapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1307 return cydriver._cuGraphicsUnmapResources(count, resources, hStream) 2VgWgXgYgZg0gni1gBr2g3gXk7f
1309cdef CUresult cuGetProcAddress(const char* symbol, void** pfn, int cudaVersion, cuuint64_t flags, CUdriverProcAddressQueryResult* symbolStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
1310 return cydriver._cuGetProcAddress_v2(symbol, pfn, cudaVersion, flags, symbolStatus)
1312cdef CUresult cuCoredumpGetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1313 return cydriver._cuCoredumpGetAttribute(attrib, value, size)
1315cdef CUresult cuCoredumpGetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1316 return cydriver._cuCoredumpGetAttributeGlobal(attrib, value, size) 2=V
1318cdef CUresult cuCoredumpSetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1319 return cydriver._cuCoredumpSetAttribute(attrib, value, size)
1321cdef CUresult cuCoredumpSetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1322 return cydriver._cuCoredumpSetAttributeGlobal(attrib, value, size) 2=V
1324cdef CUresult cuCoredumpRegisterStartCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
1325 return cydriver._cuCoredumpRegisterStartCallback(callback, userData, callbackOut)
1327cdef CUresult cuCoredumpRegisterCompleteCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
1328 return cydriver._cuCoredumpRegisterCompleteCallback(callback, userData, callbackOut)
1330cdef CUresult cuCoredumpDeregisterStartCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
1331 return cydriver._cuCoredumpDeregisterStartCallback(callback)
1333cdef CUresult cuCoredumpDeregisterCompleteCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
1334 return cydriver._cuCoredumpDeregisterCompleteCallback(callback)
1336cdef CUresult cuGetExportTable(const void** ppExportTable, const CUuuid* pExportTableId) except ?CUDA_ERROR_NOT_FOUND nogil:
1337 return cydriver._cuGetExportTable(ppExportTable, pExportTableId)
1339cdef CUresult cuGreenCtxCreate(CUgreenCtx* phCtx, CUdevResourceDesc desc, CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1340 return cydriver._cuGreenCtxCreate(phCtx, desc, dev, flags)
1342cdef CUresult cuGreenCtxDestroy(CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1343 return cydriver._cuGreenCtxDestroy(hCtx)
1345cdef CUresult cuCtxFromGreenCtx(CUcontext* pContext, CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1346 return cydriver._cuCtxFromGreenCtx(pContext, hCtx)
1348cdef CUresult cuDeviceGetDevResource(CUdevice device, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
1349 return cydriver._cuDeviceGetDevResource(device, resource, typename) 2?V
1351cdef CUresult cuCtxGetDevResource(CUcontext hCtx, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
1352 return cydriver._cuCtxGetDevResource(hCtx, resource, typename)
1354cdef CUresult cuGreenCtxGetDevResource(CUgreenCtx hCtx, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
1355 return cydriver._cuGreenCtxGetDevResource(hCtx, resource, typename)
1357cdef CUresult cuDevSmResourceSplitByCount(CUdevResource* result, unsigned int* nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, unsigned int minCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1358 return cydriver._cuDevSmResourceSplitByCount(result, nbGroups, input, remainder, flags, minCount) 2?V
1360cdef CUresult cuDevSmResourceSplit(CUdevResource* result, unsigned int nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, CU_DEV_SM_RESOURCE_GROUP_PARAMS* groupParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1361 return cydriver._cuDevSmResourceSplit(result, nbGroups, input, remainder, flags, groupParams)
1363cdef CUresult cuDevResourceGenerateDesc(CUdevResourceDesc* phDesc, CUdevResource* resources, unsigned int nbResources) except ?CUDA_ERROR_NOT_FOUND nogil:
1364 return cydriver._cuDevResourceGenerateDesc(phDesc, resources, nbResources)
1366cdef CUresult cuGreenCtxRecordEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1367 return cydriver._cuGreenCtxRecordEvent(hCtx, hEvent)
1369cdef CUresult cuGreenCtxWaitEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1370 return cydriver._cuGreenCtxWaitEvent(hCtx, hEvent)
1372cdef CUresult cuStreamGetGreenCtx(CUstream hStream, CUgreenCtx* phCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1373 return cydriver._cuStreamGetGreenCtx(hStream, phCtx)
1375cdef CUresult cuGreenCtxStreamCreate(CUstream* phStream, CUgreenCtx greenCtx, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil:
1376 return cydriver._cuGreenCtxStreamCreate(phStream, greenCtx, flags, priority)
1378cdef CUresult cuGreenCtxGetId(CUgreenCtx greenCtx, unsigned long long* greenCtxId) except ?CUDA_ERROR_NOT_FOUND nogil:
1379 return cydriver._cuGreenCtxGetId(greenCtx, greenCtxId)
1381cdef CUresult cuStreamGetDevResource(CUstream hStream, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil:
1382 return cydriver._cuStreamGetDevResource(hStream, resource, typename)
1384cdef CUresult cuLogsRegisterCallback(CUlogsCallback callbackFunc, void* userData, CUlogsCallbackHandle* callback_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1385 return cydriver._cuLogsRegisterCallback(callbackFunc, userData, callback_out)
1387cdef CUresult cuLogsUnregisterCallback(CUlogsCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
1388 return cydriver._cuLogsUnregisterCallback(callback)
1390cdef CUresult cuLogsCurrent(CUlogIterator* iterator_out, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1391 return cydriver._cuLogsCurrent(iterator_out, flags)
1393cdef CUresult cuLogsDumpToFile(CUlogIterator* iterator, const char* pathToFile, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1394 return cydriver._cuLogsDumpToFile(iterator, pathToFile, flags)
1396cdef CUresult cuLogsDumpToMemory(CUlogIterator* iterator, char* buffer, size_t* size, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1397 return cydriver._cuLogsDumpToMemory(iterator, buffer, size, flags)
1399cdef CUresult cuCheckpointProcessGetRestoreThreadId(int pid, int* tid) except ?CUDA_ERROR_NOT_FOUND nogil:
1400 return cydriver._cuCheckpointProcessGetRestoreThreadId(pid, tid)
1402cdef CUresult cuCheckpointProcessGetState(int pid, CUprocessState* state) except ?CUDA_ERROR_NOT_FOUND nogil:
1403 return cydriver._cuCheckpointProcessGetState(pid, state) 2h0
1405cdef CUresult cuCheckpointProcessLock(int pid, CUcheckpointLockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1406 return cydriver._cuCheckpointProcessLock(pid, args)
1408cdef CUresult cuCheckpointProcessCheckpoint(int pid, CUcheckpointCheckpointArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1409 return cydriver._cuCheckpointProcessCheckpoint(pid, args)
1411cdef CUresult cuCheckpointProcessRestore(int pid, CUcheckpointRestoreArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1412 return cydriver._cuCheckpointProcessRestore(pid, args)
1414cdef CUresult cuCheckpointProcessUnlock(int pid, CUcheckpointUnlockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1415 return cydriver._cuCheckpointProcessUnlock(pid, args)
1417cdef CUresult cuProfilerStart() except ?CUDA_ERROR_NOT_FOUND nogil:
1418 return cydriver._cuProfilerStart() 2@V
1420cdef CUresult cuProfilerStop() except ?CUDA_ERROR_NOT_FOUND nogil:
1421 return cydriver._cuProfilerStop() 2@V
1423cdef CUresult cuGraphicsEGLRegisterImage(CUgraphicsResource* pCudaResource, EGLImageKHR image, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1424 return cydriver._cuGraphicsEGLRegisterImage(pCudaResource, image, flags)
1426cdef CUresult cuEGLStreamConsumerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream) except ?CUDA_ERROR_NOT_FOUND nogil:
1427 return cydriver._cuEGLStreamConsumerConnect(conn, stream)
1429cdef CUresult cuEGLStreamConsumerConnectWithFlags(CUeglStreamConnection* conn, EGLStreamKHR stream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1430 return cydriver._cuEGLStreamConsumerConnectWithFlags(conn, stream, flags)
1432cdef CUresult cuEGLStreamConsumerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1433 return cydriver._cuEGLStreamConsumerDisconnect(conn)
1435cdef CUresult cuEGLStreamConsumerAcquireFrame(CUeglStreamConnection* conn, CUgraphicsResource* pCudaResource, CUstream* pStream, unsigned int timeout) except ?CUDA_ERROR_NOT_FOUND nogil:
1436 return cydriver._cuEGLStreamConsumerAcquireFrame(conn, pCudaResource, pStream, timeout)
1438cdef CUresult cuEGLStreamConsumerReleaseFrame(CUeglStreamConnection* conn, CUgraphicsResource pCudaResource, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1439 return cydriver._cuEGLStreamConsumerReleaseFrame(conn, pCudaResource, pStream)
1441cdef CUresult cuEGLStreamProducerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream, EGLint width, EGLint height) except ?CUDA_ERROR_NOT_FOUND nogil:
1442 return cydriver._cuEGLStreamProducerConnect(conn, stream, width, height)
1444cdef CUresult cuEGLStreamProducerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1445 return cydriver._cuEGLStreamProducerDisconnect(conn)
1447cdef CUresult cuEGLStreamProducerPresentFrame(CUeglStreamConnection* conn, CUeglFrame eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1448 return cydriver._cuEGLStreamProducerPresentFrame(conn, eglframe, pStream)
1450cdef CUresult cuEGLStreamProducerReturnFrame(CUeglStreamConnection* conn, CUeglFrame* eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1451 return cydriver._cuEGLStreamProducerReturnFrame(conn, eglframe, pStream)
1453cdef CUresult cuGraphicsResourceGetMappedEglFrame(CUeglFrame* eglFrame, CUgraphicsResource resource, unsigned int index, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil:
1454 return cydriver._cuGraphicsResourceGetMappedEglFrame(eglFrame, resource, index, mipLevel)
1456cdef CUresult cuEventCreateFromEGLSync(CUevent* phEvent, EGLSyncKHR eglSync, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1457 return cydriver._cuEventCreateFromEGLSync(phEvent, eglSync, flags)
1459cdef CUresult cuGraphicsGLRegisterBuffer(CUgraphicsResource* pCudaResource, GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1460 return cydriver._cuGraphicsGLRegisterBuffer(pCudaResource, buffer, Flags) 2VgLoWgXgMo(V)V*V+V,VYgZg0gni1gBr2g.V3gXk7f/V:V;V
1462cdef CUresult cuGraphicsGLRegisterImage(CUgraphicsResource* pCudaResource, GLuint image, GLenum target, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1463 return cydriver._cuGraphicsGLRegisterImage(pCudaResource, image, target, Flags) 2-V
1465cdef CUresult cuGLGetDevices(unsigned int* pCudaDeviceCount, CUdevice* pCudaDevices, unsigned int cudaDeviceCount, CUGLDeviceList deviceList) except ?CUDA_ERROR_NOT_FOUND nogil:
1466 return cydriver._cuGLGetDevices_v2(pCudaDeviceCount, pCudaDevices, cudaDeviceCount, deviceList)
1468cdef CUresult cuVDPAUGetDevice(CUdevice* pDevice, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1469 return cydriver._cuVDPAUGetDevice(pDevice, vdpDevice, vdpGetProcAddress)
1471cdef CUresult cuVDPAUCtxCreate(CUcontext* pCtx, unsigned int flags, CUdevice device, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1472 return cydriver._cuVDPAUCtxCreate_v2(pCtx, flags, device, vdpDevice, vdpGetProcAddress)
1474cdef CUresult cuGraphicsVDPAURegisterVideoSurface(CUgraphicsResource* pCudaResource, VdpVideoSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1475 return cydriver._cuGraphicsVDPAURegisterVideoSurface(pCudaResource, vdpSurface, flags)
1477cdef CUresult cuGraphicsVDPAURegisterOutputSurface(CUgraphicsResource* pCudaResource, VdpOutputSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1478 return cydriver._cuGraphicsVDPAURegisterOutputSurface(pCudaResource, vdpSurface, flags)