Coverage for cuda/bindings/cydriver.pyx: 68.12%
1029 statements
« prev ^ index » next coverage.py v7.15.0, created at 2026-07-03 01:38 +0000
« prev ^ index » next coverage.py v7.15.0, created at 2026-07-03 01:38 +0000
1# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved.
2#
3# SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE
4#
5# This code was automatically generated across versions from 12.9.0 to 13.3.0, generator version 0.3.1.dev1622+g48467ab08.d20260421. Do not modify it directly.
7from ._internal cimport driver as _driver
9cdef CUresult cuGetErrorString(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil:
10 return _driver._cuGetErrorString(error, pStr) 2`M4y{M
13cdef CUresult cuGetErrorName(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil:
14 return _driver._cuGetErrorName(error, pStr) 2Js4lKs5l6l{b7l`M4y{MR1|M}M~MaNbNcbNhnj
17cdef CUresult cuInit(unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
18 return _driver._cuInit(Flags) 2a 8l5yLs6y7y8y9y!y#y$y%y'y(y)y*y+y,y-y.y/y:yMsNsOsPsQsRsSsTsUsIqVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s;y=y?y@y[y]y^y_y`y{y|y}y~yazbzXcczdzezfz
21cdef CUresult cuDriverGetVersion(int* driverVersion) except ?CUDA_ERROR_NOT_FOUND nogil:
22 return _driver._cuDriverGetVersion(driverVersion) 2a S1T1U1V1W1X1
25cdef CUresult cuDeviceGet(CUdevice* device, int ordinal) except ?CUDA_ERROR_NOT_FOUND nogil:
26 return _driver._cuDeviceGet(device, ordinal) 25y6y7y8y9y!y#y$y%y'y(y)y*y+y,y4y-y.y/y:yMsNsOsPsQsRsSsTsUsIqVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s;y=y?y@y[y]y^y_y`y{y|y}y~yazbzczdzezfz
29cdef CUresult cuDeviceGetCount(int* count) except ?CUDA_ERROR_NOT_FOUND nogil:
30 return _driver._cuDeviceGetCount(count) 2a %scNdNeNfNgNhNiNjNkNlNmNnNoNpNqNrNsNtNuNvNwNxNyNzNANBNCNDNENFNGNHNINJNKNLNMNNNONPNQNgzhzizjzY1kzlzmznzoz9loj!lpzpj#l$lqzrzsztzuzRNvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z%l'l|bqjbecerj(l)l*l+lxddeOhPhQhRh,l-l.l/l}bsjeefetj:l;l=l?lydgeShThUhVh@l[l]luj^l4zvj_l`l{lwj|lxj}l~lambm~byjheiezjcmdmemfmzdjeWhXhYhZhgmhmimjmacAjkeleBjkmlmmmnmAdme0h1h2h3hompmqmrmbcneoeCjsmtmumvmBdpe4h5h6h7hwmxmymzmccDjqereEjAmBmCmDmCdse8h9h!h#hEmFmGmFjHmGjImJmKmHjLmIjMmNmSNOmJjPmKjQmRmTNUNVNWNXNYNZN0N1N2N3N4N5N6N7N8N9N!N#N$N%N'N(N)N*N+N,N-N.N/N:N;N=N?N@N[N]N^N_N`N{N|N}N~NaObOcOdOeOfOgOhOiOjOkOlOmOnOoOpOqOrO5z6zsOtOuOvOwOxOyOzOAOJqBO'sKqSmLqMqNqOqPqQqRqCOTmLj(sUmMjVmNj)sSqTqUqVqWqXqYqZq0qDOEO7z8z9z!z1q#z$z%z'zte(zue)z*z+z) OjdbPjlg,z-z.z/z:z;z=z?z@z[z]z^z_z`z{z|z}z~zaAbAcAdAeAmgQjfAgAhA2qve3q$hngRjZ1ebfb. VbWbXb%h'h4qgbhbibjbkblbLsFOGOHOIOJOKOLOMO*s+s,s-s.s/s:s;s=s?s@s[sNO]sYc3 ZcOOWmPOQOROSOTOUOVOWOXOYOZO0OSjiATjUjweXmYmVjWjXj1OYjZj0jjAkAlAmAnAoApAqArAsAtAuAvAwAxAyAzAAA2Oxedc0c1c2c^s_s`s{s|s}s~satbtctdtetftgthtitjtktltmtntotptqtrtstttutvtwtxtytztAtogZm0mpg5q6qBtCtDtEtFtGtHtItJtKtLtMtNtOtPtQtRtStTtUtVtWtXtYtZt0t1t2t3t4t5t6t7t8t9t!t#t$t%t'tBAYb01(tCA3O3c4O5O(h)h*h6Omb7ODd8O+hyeEd9O4c,h!Oze-hAe.h#Oqg/h$OBeFd%Oec:hCe;h5crg'O(Osgtgug)O*O6c+Ovg=hDe,OGd-Ofc?hEe@h.OFe[h/OGe1jHeHd:Ogc]hIewgxg^hJe7cId2jDA)t1m_hKeZbhcLe2m;O`h{h0bcb11=O3m4m5m?O6m7m8mO @O9mNh[O]O^O_O`O{O|O}O~OaP!m#m$m%m*t+t,t-t.t/t:t;tbPcP'm(m)m*m+m,m-m.m/m:m;m=m?m@m[m]m^m_m`m{m|m}m~manbncndnenfngnhninjnknlnmnnnonpnqnrnsntnunvnwnxnynznAnBnCnDnEnFnGnHnInJnKnLnMnNnOnPnQnRnSnTn=tUn3jic7qdPeP4jEA5j6j7jFAVnWnXnYnMeNe|h8qGA?tZn8j0n@t1n9jjc9qfPHA!jIA#j$j%jJA2n3n4nOePe}h!qKA[t5n6n1bQeRe'jygzgAgJdSe~hBgCgTe* UeKd8c9cLdaiMdNdOdVenb(j2b!cDgbiPdQdobpb3b/ : ; = ciqbEgFgGgdi7n8n#cRdHg#q9n!n#n)jkc$q*j+j,j-jLA$n%n'n(nWegPXeei%qMA)n*n.jfi4b+nNAgi]thiiiji^t/j:j;j=jSdOATdIg,n_t'q?j@j[jrbUdVdkiYeZe0e$c1eJg2e3e]jli5b-nPAmi^j_jni`t`j{j|j}jWdQAXdKg.n{t~jakoipi4e5e6e7eqi8e9e!e#esbYdZd$e%e'e0dLg(e)e/nlc(qbkckdkek:n;n=n*e+eriRA?n@nMgNgOgPg[n]n^n_n`nsimcQgRg1d2dSgfk,e-e.e/e%c:egk;e=enc'c(c)c3docpctbqcrcsc{ntc)qhkikjkkkSA|n}n~nao?e@eti*qTAboco6 6b7buc*c+c,c-c? .c/c4d[e]e5d^e_elkvcuivi`e{ewidoTgUgVgeo|e6dWgfoXgYggowcmknkokhoiojo}e~exikoloyiZgubpk|t0g+q1g2g3g,qziAiBiCi:c}t;cafqk-qDiEimonorkxc.qhPiPskUAtkukvkVAoopoqorobfcfFi/qWA~tsoto8bdfefwk4g5g6g7dffGi7g8ggf+ hf8d=c?c9dHi!d#d$dif9bxk!b@cIiJi%d'dvbwb#b@ [ ] ^ Kixb9g!g#g$gLiuovo[c(d%g:qwoxoyoykyc;qzkAkBkCkXAzoAoBoCojfjPkfMiauYADoEoFoDkzc=qkPEkZAFkGkHk0AGoHoIoJolflPmfNibu1AcuKoLoIkyb)d*dOinfofpf]cqf'grfsfJkPi$bMo2AQiKkLkRiduMkNkOkPk+d3A,d(g?qeuQkRkSiTitfufvfwfUixfyfzfAfzb-d.dBfCfDf/d)gEfFfNoAc@qSkTkUkVkOoPoQoGfHfVi4ARoSo*g+g,g-gToUoVoWoXoWiBc.g/g:d;d:gWkIfJfKfLf^cMfXkNfOfCc_c`c{c=dDcEcAbFcGcHcYoIc[qYkZk0k1k5AZo0o1o2oPfQfXifu6A3o4o7 %b'bJc|c}c~cad_ bdcd?dRfSf@dTfUf5oKc2k3k;g=g4k]qYiZi0i6oVfWf1i^q2i3i7oLc5k6k7k8k8o9o!oXfYf4i#o$o5i?gBb9kgu@g_q[g]g^g`q6i7i8i9iddhuedZf%o{q!i#i'omPnPfdgdXc[diuju(o!kMc|qoP7A#k8A$k%k'k9A)o*o+o,o0f1f$i}q~qpPkuluqP!Amu-o.o/o(kNcarrPsP)k#A*k+k,k$A:o;o=o?o2f3f%ibr%Anu@o[o]o-kOccrtP'A.k(A/k:k;k)A^o_o`o{o4f5f'idr*Aou|o}o~o=kPceruP+A?k,A@k[k]k-Aapbpcpdp6f7f(ifr.Apuepfpgp^kQcgrvP/A_k:A`k{k|k;Ahpipjpkp8f9f)ihr=Aqulpmpnp}kRcirwP?A~k@Aalblcl[Aopppqprp!f#f*ijr]ArusptpupdlSckrxPyPel^Aflglhl_Avpwpxpyp$f%f+isutu`AuuzpApBpilTclrzPAPjl{Aklllml|ACpDpEpFp'f(f,ivuwu}AxuGpHpBPCPyuDPEPFPGPHPIPJPKPLPMPNPOPPPQPRPSPTPUPVPWPXPYPZP0P1P2P3P4P5P6P7P8P9P!P#P$P%PzuAunj'P(P)P*P+P,P-P.P/P:PBuCuDuEuFu;PGuHuIuJuKu=P?P@P[P]P^P_P`P{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQqQrQsQtQLuMuNuOuPuQuRuSuTuUuVuWuXuYuZu0u1u2u3u4u5u6u7u8u9u!u#u$u%u'u(u)u*u+u,u-u.u/uuQvQwQ:u;u=uxQyQzQAQBQCQDQEQFQGQHQIQJQKQLQMQNQOQPQQQRQSQTQUQVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!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~QaRbRcRdReRfRgRhR)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}f~fagbgcgiRjRkRlRmRnRoRpRqRrRsRtRuRvRwRxRyRzRARBRCRDR
33cdef CUresult cuDeviceGetName(char* name, int len, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
34 return _driver._cuDeviceGetName(name, len, dev) 2SmEO21IpJp1q?u@u[uteue) ` KpLpMpdbNp-iOpPpPjlg2q]u^uve3q$hng.iebfb. VbWbXb%h'h4q_uLsER~A7A
37cdef CUresult cuDeviceGetUuid(CUuuid* uuid, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
38 return _driver._cuDeviceGetUuid_v2(uuid, dev) 2SmMqOqOjmrQjRj314151617181]saBye4czeAeqgBeecCeDefcEeFeGeHegcIewghc`h{h=tHA.jfi4b+nNAgi]thiiiji^t/j:j;j=jSdOATdIg,n_t'q?j@jfdgdXc[d'A+A/A?A
41cdef CUresult cuDeviceGetLuid(char* luid, unsigned int* deviceNodeMask, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
42 return _driver._cuDeviceGetLuid(luid, deviceNodeMask, dev)
45cdef CUresult cuDeviceTotalMem(size_t* bytes, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
46 return _driver._cuDeviceTotalMem_v2(bytes, dev)
49cdef CUresult cuDeviceGetTexture1DLinearMaxWidth(size_t* maxWidthInElements, CUarray_format format, unsigned numChannels, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
50 return _driver._cuDeviceGetTexture1DLinearMaxWidth(maxWidthInElements, format, numChannels, dev)
53cdef CUresult cuDeviceGetAttribute(int* pi, CUdevice_attribute attrib, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
54 return _driver._cuDeviceGetAttribute(pi, attrib, dev) 2a %sU (b{ V Uc8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L bBcBnrJs`udB{u9loj!lpj#l$lorhdidjd]d5 91!1DbEbFb*bGb9 ! # - +b,b-bVc#1prqrrrsrtrur/inl%l'l|bqjbecerjxddeOhPhQhRh.l/l}bsjeefetjydgeShThUhVh]luj^lvj_l`l{lwj|lxj}l~lambm~byjheiezjzdjeWhXhYhZhimjmacAjkeleBjAdme0h1h2h3hqmrmbcQpneoeCjBdpe4h5h6h7hymzmccDjqereEjCdse8h9h!h#hGmFjHmGjImJmKmHjLmIjMmNmOmJjPmKjQmRm$1olvr^d%1kd'1FRGRHRIRJRHbIbJbKb.b_d`dM P wrdg0 | } /bQ N A B C b $ x 5z6zG 1 2 Lb:b;bld=bW Jq8lKqLqNqPqQqRqxrTmLj(sUmMjVmNj)sSqTqUqVqWqXqYqZq0q) ` OjmryrQjRjLsRpeBfB_g`ggBhBiBjBkBlBmBnBoBpBqBrBsBtBuBvBwBxB*syBzBABBBCBDBEBFB+sGBHBIBJBKBLBMBNBOBPBQBRBSBTB,sUB-sVBWBXBYBZB0B1B2B3B4B5B6B7B8B9B!B#B$B%B'B(B)B*B+B,B-B.B/B:B;B=B?B@B[B]B^B_B.s`B{B|B}B~B/saCbCcCdCeCfCgChC:siCjCkClCmC;snCoCpCqCrCsCtCuC=svCwCxCyCzCACBCCCDCECFCGCHCICJCKCLC?sMC@sNCOCPC[sQCRCSCTCUCVC3 ~ WcMbweX XmY Ym(1)1Nb{d|d:i;i=ieg?i@idc0c1c2cfg^s_s`s{s|s}s~satbtctWCdtetftgthtitjtktltmtntotptqtrtstttutvtwtxtytztXCAt[ipg]i^iKRYbCApl3c|uql}u(h)h*h~umb_iDdrl+hyeEd,hze-hAe.h/hBeFdec:hCeYC5cZCrg0Csg1Ctg2Cug3C6c4Cvg5C=hDeGdfc?hEe@hFe[hGeHeHdgc]hIewgxg^h7cIdDA{gKeslZbhcLe2m`h{hLRmd0bcbMRnd6CNR3m4m5mzr6m7m8mO 9mNhArBrCrDrErFrGrHrIrJr!m#m$m%m*t+t,t-t.t/t:t;t*1+17C'm8C(m9C)m!C*m#C+m$C,mav-mbv.mcv/mdv:mev;mfv=mgv?mhv@miv[mjv]mkv^mlv_mmv`mnv{mov|mpv}mqv~mrvanbncn%Cdn'Cen(Cfn)Cgn*Chn+Cin,Cjn-Ckn.Cln/Cmn:Cnn;Con=Cpn?Cqn@Crn[Csn]Ctn^Cun_Cvn`Cwn{CxnynznAnBnCnDnEnFnGnHnInJnKnLnMnNnOnPn=tUn3jic4j7jYnMeNe|h8q8j0n1n9jjc!j%j4nOePe}h!q1bQeRe'jygzgAgJdSe~hBgCgTe* UeKd8c9cLdaiMdNdOdVenb(j2b!cDgbiPdQdobpb3b/ : ; = ciqbEgGg#cRdHg#n)jkc*j-j(nWeXeei%q.jfi4bgiji=jSdTdIg,n[jrbUdVdkiYeZe0e$c1eJg2e3e]jli5bmini}jWdXdKg.nsbYdZd$e%e'e0dLg(e)e/nlcbkek*e+erisimcQgRg1d2dSgfk,e-e.e/e%c:egk;e=enc'c(c)c3docpctbqcrcsc{ntchkkkao?e@eti*q6 6b7buc*c+c,c-c? .c/c4d[e]e5d^e_elkvcuivi`e{ewidoTgUgVgeo|e6dWgfoXgYggowcmkok}e~exiyiZgub0g3gCi:c;cafqknorkxcskvkrobfcfFi/q8bdfefwk4g5g6g7dffGi7g8ggf+ hf8d=c?c9dHi!d#d$dif9bxk!b@cIiJi%d'dvbwb#b@ [ ] ^ Kixb9g$g[c(d%gyoykyczkCkCojfkfMiauFoDkzcEkHkJolfmfNibuIkyb)d*dOinfofpf]cqf'grfsfJkPi$bQiRiPk+d,d(g?qzb-d.dBfCfDf/d)gEfFfNoAcSkVkGfHfViWiBc.g/g:d;d:gWkIfJfKfLf^cMfXkNfOfCc_c`c{c=dDcEcAbFcGcHcYoIcYk1k2oPfQfXifu7 %b'bJc|c}c~cad_ bdcd?dRfSf@dTfUf5oKc2k3k;g=g4k]qYiZi0i6oVfWf1i^q2i3i7oLc5k8kXfYf4i5i?gBb@g^g9iddedZf%ofdgdXc[diuju(o!kMc#k'k,o0f1f$i}q~qkulu/o(kNc)k,k?o2f3f%ibr]o-kOc.k;k{o4f5f'idr~o=kPc?k]kdp6f7f(ifrgp^kQc_k|kkp8f9f)ihrnp}kRc~kclrp!f#f*ijrupdlScelhlyp$f%f+isutuBpilTcjlmlFp'f(f,ivuwuORPRyuQRRRSRTRzuAunjBuCuDuEuFuURGuHuIuJuKuLuMuNuOuPuQuRuSuTuUuVuWuXuYuZu0u1u2u3u4u5u6u7u8u9u!u#u$u%u'u(u)u*u+u,u-u.u/u:u;u=uZ odtlulvlwlxlylzlAlBlClDlEl|g}g)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}f~fagbgcgSpTp
57cdef CUresult cuDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, CUdevice dev, int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
58 return _driver._cuDeviceGetNvSciSyncAttributes(nvSciSyncAttrList, dev, flags)
61cdef CUresult cuDeviceSetMemPool(CUdevice dev, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
62 return _driver._cuDeviceSetMemPool(dev, pool) 2VR
65cdef CUresult cuDeviceGetMemPool(CUmemoryPool* pool, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
66 return _driver._cuDeviceGetMemPool(pool, dev) 2M P ?b@b[by $ z x D abE F _g`gMbX Y [ipg]i^iBA|C_i{gO 3j8j9jTe* UeKd8c9cLdaiMdNdOdVenb(j2b!cDgbiPdQd)jfiliZgrkgf+ hf8d=c?c9dHi!d#d$dif9bxk!b@cIiJi%d'dykDkPi?g!k(k-k=k^k}kdlilZ odtlulvlwlxlylzlAlBlClDlEl|g}g)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}f~fagbgcgSpTp
69cdef CUresult cuDeviceGetDefaultMemPool(CUmemoryPool* pool_out, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
70 return _driver._cuDeviceGetDefaultMemPool(pool_out, dev) 2VR
73cdef CUresult cuDeviceGetExecAffinitySupport(int* pi, CUexecAffinityType type, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
74 return _driver._cuDeviceGetExecAffinitySupport(pi, type, dev)
77cdef CUresult cuFlushGPUDirectRDMAWrites(CUflushGPUDirectRDMAWritesTarget target, CUflushGPUDirectRDMAWritesScope scope) except ?CUDA_ERROR_NOT_FOUND nogil:
78 return _driver._cuFlushGPUDirectRDMAWrites(target, scope)
81cdef CUresult cuDeviceGetProperties(CUdevprop* prop, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
82 return _driver._cuDeviceGetProperties(prop, dev)
85cdef CUresult cuDeviceComputeCapability(int* major, int* minor, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
86 return _driver._cuDeviceComputeCapability(major, minor, dev)
89cdef CUresult cuDevicePrimaryCtxRetain(CUcontext* pctx, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
90 return _driver._cuDevicePrimaryCtxRetain(pctx, dev) 28lMsNsOsPsQsRsSsTsUsIqVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s
93cdef CUresult cuDevicePrimaryCtxRelease(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
94 return _driver._cuDevicePrimaryCtxRelease_v2(dev) 2,1-1.1/1:1;1=1?1@1Iq[1]1^1_1`1{1|1}1~1a2b2c2d2e2f2g2h2i2j2
97cdef CUresult cuDevicePrimaryCtxSetFlags(CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
98 return _driver._cuDevicePrimaryCtxSetFlags_v2(dev, flags)
101cdef CUresult cuDevicePrimaryCtxGetState(CUdevice dev, unsigned int* flags, int* active) except ?CUDA_ERROR_NOT_FOUND nogil:
102 return _driver._cuDevicePrimaryCtxGetState(dev, flags, active)
105cdef CUresult cuDevicePrimaryCtxReset(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
106 return _driver._cuDevicePrimaryCtxReset_v2(dev)
109cdef CUresult cuCtxCreate(CUcontext* pctx, CUctxCreateParams* ctxCreateParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
110 return _driver._cuCtxCreate_v4(pctx, ctxCreateParams, flags, dev) 25y6y7y8y9y!y#y$y%y'y(y)y*y+y,y-y.y/y:y;y=y?y@y[y]y^y_y`y{y|y}y~yazbzczdzezfz
113cdef CUresult cuCtxDestroy(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
114 return _driver._cuCtxDestroy_v2(ctx) 2k2l2m2n2o2p2q2r2s2t2u2v2w2x2y2z2A2B2C2D2E2F2G2H2I2J2K2L2M2N2O2P2Q2R2S2T2U2V2
117cdef CUresult cuCtxPushCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
118 return _driver._cuCtxPushCurrent_v2(ctx) 2}CWR
121cdef CUresult cuCtxPopCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
122 return _driver._cuCtxPopCurrent_v2(pctx) 2XRYRZR0R1R2R3R4R5R6R7R8R9R!R#R$R%R'R(R)R*R+R,R-R.R/R:R;R=R?R@R[R]R^R_R`R{R|R}R~RaSbScS~CaDbDcDdDeDfDgDhDiDjDkDlDmDnDoDpDqDrDsDtDdSuDvDwDxDyDsvzDADeSfSBDCDDDEDFDGDHDIDJDKDLDMDNDgSODPDQDRDSDTDUDVDWDXDYDZD0D1DhStvuv2D3DiS4D5D6D7D8D9D!D#D$D%D'D(D)DjSvvwv*D+DkS,D-D.D/D:D;D=D?D@D[D]D^D_D`D{D|D}D~DaEbEcEdEeEfEgEhEiExvyvjEkElEmEnEoEpEqErEsEtEuEvEwExEyEzEzvAvAEBECEDEEEFEGEHEIEJEKELEMENEOEPEQEBvCvRESETEUEVEWEXEYEZE0E1E2E3E4E5E6E7EDvEv8E9E!E#E$E%E'E(E)E*E+E,E-E.E/E:E;E=E?E@E[E]E^E_E`ElS{E|E}E~EaFbFmSnSoSpSqSrSsStSuSvSwSxSySzSASBSCSDSESFSGSHSISJSKSLSMSNSOSPSQSRSSSTSUSVSWSXSYSZS0S1S2S3S4S5S6S7S8S9S!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}S~ScFdFeFfFgFaTbThFiFcTjFkFlFmFdTnFoFeTfTgThTiTjTkTlTmTnToTpTqTrTsTtTuTvTwTxTyTzTATBTCTDTETFTGTHTITJTKTLTMTNTOTPTQTRTSTTTUTVTWTXTYTZT0TpFqFrF1T2T}CsFtFuF3TvFWRwFxF4T5T6T7T8T9T!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~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHUIUJUKULUMUNUOUPUQURUSUTUUUVUWUXUYUZU0U1U2U3U4U5U6U7U8U9U!U#U$U%U'U(U)U*U+U,U-U.U/U:U;U=U?U@U[U]U^U_U`U{U|U}U~UaVbVcVdVeVfVgVhViVjVkVlVmVnVoVpVqVrVsVtVuVvVwVxVyVzVAVBVCVDVEVFVGVHVIVJVKVLVMVNVOVPVQVRVSVTVUVVVWVXVYVZV0V1V2V3V4V5V6V7V8V9V!V#V$V%V'V(V)V*V+V,V-V.V/V:V;V=V?V@V[V]V^V_V`V{V|V}V~VaWbWcWdWeWfWgWhWiWjWkWlWmWnWoWpWqWrWsWtWuWvWwWxWyWzWyFzFAFBFAWBWCFDFFvGvEFFFGFHFIFCWJFKFLFDWMFNFOFPFQFEWRFSFTFUFVFFWGWWFXFHvIvYFZF0F1F2FHW3F4F5FIW6F7F8F9F!FJvKv#F$F%F'F(F)F*F+F,FLvMvNvOvKrLrPvQvRvSvTv-FUv.FVvWv/FXvYvZv0v1v:F;F=F?F@F[F]F^F2v3v_F`F{F|F}F~FaGbGcGdGeGfGgGhGiG4v5vjGkGlGmGnGJWoGKWpGqGLWrGsGtGuGvGwGxGMWyGzG6v7vAGBGCGDGEGNWFGOWGGHGPWIGJGKGLGMGNG8v9vOGPGQGRGSGTGUGVGWG!v#v$v%vXG'v(v)v*v+v,v-v.vYG/vZG:v;v0G=v?v@v[v]v^v_v`v{v|v}v~vawbw1Gcwdw2G3G4G5G6G7G8G9G!G#G$Gewfw%G'G(G)G*G+G,G-G.G/G:G;G=G?G@G[G]G^G_G`G{G|G}Ggwhw~GaHbHcHdHeHfHgHhHiHjHkHiwjwlHmHnHoHpHqHrHsHtHuHvHwHkwlwxHyHzHAHBHQWCHDHEHRWFHGHHHIHmwnwJHKHLHMHNHOHowpwPHQHRHSHTHUHVHWHXHYHqwrwZH0H1H2H3HSW4H5H6H7H8H9H!H#H$Hswtw%H'H(H)H*H+H,H-H.Huwvwwwxw/HywzwMrNrAwBwCwDwEw:HFw;HGwHw=HIwJwKw?H@H[H]H^HTWUW_H`HLwMw{H|H}H~HaIVWbIcIdIWWeIfIgIhIiINwOwjIkIlImInIoIpIqIrIPwQwRwSwOrPrTwUwVwWwXwsIYwtIZw0wuI1w2w3w4w5wvIwIxIyIzIAIBICI6w7wDIEIFIGIHIIIJIKILIMINIOIPIQIRI8w9wSITIUIVIWIXWXIYWYIZIZW0I1I2I3I4I5I6I0W7I8I!w#w9I!I#I$I%I1W'I2W(I)I3W*I+I,I-I.I/I$w%w:I;I=I?I@I[I]I^I_I'w(w)w*w`I+w,w-w.w/w:w;w=w{I?w|I@w[w}I]w^w_w`w{w|w}w~waxbxcxdxexfx~IgxhxaJbJcJdJeJfJgJhJiJjJkJixjxlJmJnJoJpJqJrJsJtJuJvJwJxJyJzJAJBJCJDJEJFJGJHJkxlxIJJJKJLJMJNJOJPJQJRJSJTJmxnxUJVJWJXJYJZJ0J1J2J3J4J5Joxpx6J7J8J9J!J4W#J$J%J5W'J(J)J*Jqxrx+J,J-J.J/J:Jsxtx;J=J?J@J[J]J^J_J`J{Juxvx|J}J~JaKbK6WcKdKeKfKgKhKiKjKkKwxxxlKmKnKoKpKqKrKsKtKyxzxAxBxuKCxDxQrRrExFxGxHxIxvKJxwKKxLxxKMxNxOxyK7W8W9W!WzKAKBKCK#W$WDKEKPxQxFKGKHKIKJK%WKKLKMK'W(W)W*W+W,WNKOKPKQKRKSKTKUK-W.WVKWKRxSxXKYKZK0K1K/W2K3K4K:W5K6K7K8K9K!K#K$K;W=W%K'KTxUx(K)K*K+K,K?W-K.K/K@W:K;K=K?K@K[K]K^K[W]W_K`KVxWx{K|K}K~KaL^WbLcLdL_WeLfLgLhLiLjLkLlL`W{WmLnLXxYxoLpLqLrLsL|WtLuLvL}WwLxLyLzLALBLCLDL~WaXELFLZx0xGLHLILJLKLbXLLMLNLcXOLPLQLRLSLTLULVLdXeXWLXL1x2xYLZL0L1L2LfX3L4L5LgXhX6L7L8L9L!L#L$L%LiXjX'L(L3x4x)L*L+L,L-LkX.L/L:LlXmX;L=L?L@LnXoXpXqXrXsXtXuXvXwXxXyXzXAXBXCXDXEXFXGXHXIXJXKXLXMXNXOXPXQXRXSXTXUXVXWXXXYXZX0X1X2X3X4X5X6X7X8X9X!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~XaYbYcYdYeYfYgYhYiYjYkYlYmYnYoYpYqYrYsYtYuYvYwYxYyYzYAYBYCYDYEYFYGYHYIYJYKYLYMYNYOYPYQYRYSYTYUYVYWYXYYYZY0Y1Y2Y3Y4Y5Y6Y7Y8Y9Y!Y#Y$Y%Y'Y(Y)Y*Y+Y,Y-Y.Y/Y:Y;Y=Y?Y@Y[Y]Y^Y_Y`Y{Y|Y}Y~YaZbZcZdZeZfZgZhZiZjZkZlZmZnZoZpZqZrZsZtZuZvZwZxZyZzZAZBZCZDZEZFZGZHZIZJZKZLZMZNZOZPZQZRZSZTZUZVZWZXZYZZZ0Z1Z2Z3Z4Z5Z6Z7Z8Z9Z!Z#Z$Z%Z'Z(Z)Z*Z+Z,Z-Z.Z/Z:Z;Z=Z?Z@Z[Z]Z^Z_Z`Z{Z|Z}Z~Za0b0c0d0e0f0g0h0
125cdef CUresult cuCtxSetCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
126 return _driver._cuCtxSetCurrent(ctx) 2W2cNdNeNfNgNhNiNjNkNlNmNnNoNpNqNrNsNtNuNvNwNxNyNzNANBNCNDNENFNX2GNHNINJNKNLNMNNNONPNQNgzhzizjzkzlzmznzoz9loj!lpzpj#l$lqzrzsztzuzRNvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z%l'l|bqjbecerj(l)l*l+lxddeOhPhQhRh,l-l.l/l}bsjeefetj:l;l=l?lydgeShThUhVh@l[l]luj^l4zvj_l`l{lwj|lxj}l~lambm~byjheiezjcmdmemfmzdjeWhXhYhZhgmhmimjmacAjkeleBjkmlmmmnmAdme0h1h2h3hompmqmrmbcQpneoeCjsmtmumvmBdpe4h5h6h7hwmxmymzmccDjqereEjAmBmCmDmCdse8h9h!h#hEmFmGmFjHmGjImJmKmHjLmIjMmNmSNOmJjPmKjQmRmTNUNVNWNXNYNZN0N1N2N3N4N5N6N7N8N9N!N#N$NY2%N'N(N)N*N+N,N-N.N/N:N;N=N?N@N[N]N^N_N`N{N|N}N~NaObOcOdOeOfOgOhOiOjOkOlOmOnOoOpOqOrOZ202122232425262728292!2#2$2%2'2(2)2*2+25z,2-2.2/26zsOtOuOvOwOxOyOzOAOJq8lBOKqLqNqPqQqRqxrCOTmLj(sUmMjVmNj)sSqTqUqVqWqXqYqZq0q`iDO[L5x]L6x^L7x_L8x`L9x{L!x|LOj:2;2=2?2@2[2]2^2_2`2{2Pjmrlgyr}L#x~LaMbMcMdMeMfMgMhMiMjMkM$x%x'x(x)x*x+x,x-xQj.x/xlM:xmM;xnM=xoMRjebpMfb?x|2}2qM@xrM[xsM]x~2a3b3c3d3e3FOf3GOHOIOJOKOMsNsOsPsQsRsSsTsUsIqVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s_g`gg3LOh3i3j3MOk3l3m3n3ERtMo3NOYc3 ZcOOWmPOp3QOROSOTOUOVOq3WOXOr3s3YOZO0O~gUpahbhSjchdheh{ifhghhhFliATjUjweXmYmVjWjXj1OYjZj0jjAkAlAmAnAoApAqArAsAtAuAvAwAxAyAzAAA2ONb|ixedct3u3v3w3ihjhkh0c1clhmhnhoh2cphqhrhshfgthuhvhwhxhyhzhAhBhChDhEhFhGhHh^s_s`s{s|s}s~satbtctWCdtetftgthtitjtktltmtntotptqtrtstttutvtwtxtytztXCAtog}d~dZmi0SrTr0m[ipg5q^x_x`x6q{xj0k0l0m0n0o0p0q0BtCtr0uMDts0EtFtt0u0Gtv0w0x0y0Htz0ItJtA0B0C0KtD0E0LtMtF0NtG0H0OtPtQtI0J0K0RtL0M0N0O0StP0Q0TtUtR0S0VtWtXtYtT0U0V0Zt0tW01tX02tvM3tY04tZ05t00106t7t8t209t!t30#t4050$t6070%t8090!0#0't$0%0Gl]i^iKRYbx3y3CA3Oz3pl3c|u4Oql5O}uA3(hB3)hC3*h6O~uD3mb7O_iE3Dd8OrlF3+hG3yeH3Ed9O4cI3,h!OzeJ3-hK3AeL3.h#OqgM3/h$OBeN3Fd%OecO3:hP3CeQ3;hR3S35cT3U3rg'O(OsgV3W3tgX3Y3ug)O*O6c+OZ3vg0313=h23De,OGd-Ofc33?h43Ee53@h.OFe63[h/OGe731j83He93Hd:Ogc!3]h#3Ie$3wg%3xg'3^h(3Je)37c*3Id+3DA)t|x1m_h{gKesl,3Zb-3hcLe;O.3/3:3;3=3md0bcb?3nd6C=O3m4m@35m?O6m7m8m@O9m[O]O^O_O`O{O|O}O~OaP!m#m$m%m*t+t,t'0-t.t/t:t;tbPcP'm(m)m*m+m,m-m.m/m:m;m=m?m@m[m]m^m_m`m{m|m}m~manbncndnenfngnhninjnknlnmnnnonpnqnrnsntnunvnwnxnynznAnBnCnDnEnFnGnHnInJnKnLnMnNnOnPnQn[3Rn]3Sn^3}i_3Tn=tUn3jic7qdPeP4jEA5j6j7jFAVnWnXnYnMeNe|h8qGA?tUrZn8j0n@t1n9jjc9qfPHA!jIA#j$j%jJA2n3nVr4nOePe}h!qKA[t5n6n1bQeRe'jygzgAgJdSe~hBgCgTe* UeKd8c9cLdaiMdNdOdVenb(j2b!cDgbiPdQdobpb3b/ : ; = ciqbEg~iFgGgdi7n8n#cRdHg#q9n!n#n)jkc$q*j+j,j-jLA$n%n'n(nWegPXeei%qMA)n*n.jfi4b+nNAgi]thiiiji^t/j:j;j=jSdOATdIg,n_t'q?j@j[jrbUdVdkiYeZe0e$c1eJg2e3e]jli5b-nPAmi^j_jni`t`j{j|j}jWdQAXdKg.n{t~jakoipi4e5e6e7eqi8e9e!e#esbYdZd$e%e'e0dLg(e)e/nlc(qbkckdkek:n;n=n*e+eriRA?n@nMgNgOgPg[n]n^n_n`nsimcQgRg1d2dSgfk,e-e.e/e%c:egk;e=enc'c(c)c3docpctbqcrcsc{ntc)qhkikjkkkSA|n}n~nao?e@eti*qTAboco6 6b7buc*c+c,c-c? .c/c4d[e]e5d^e_elkvcuivi`e{ewidoTgUgVgeo|e6dWgfoXgYggowcmknkVpokhoiojo}e~exikoloyiZgubpk|t0g+q1g2g3g,qziAiBiCi:c}t;cafqk-qDiEimonorkxc.qhPiPskUAtkukvkVAoopoqorobfcfFi/qWA~tsoto8bdfefwk4g5g6g7dffGi7g8ggf+ hf8d=c?c9dHi!d#d$dif9bxk!b@cIiJi%d'dvbwb#b@ [ ] ^ Kixb9g!g#g$gLiuovo[c(d%g:qwoxoyoykyc;qzkAkBkCkXAzoAoBoCojfjPkfMiauYADoEoFoDkzc=qkPEkZAFkGkHk0AGoHoIoJolflPmfNibu1AcuKoLoIkyb)d*dOinfofpf]cqf'grfsfJkPi$bMo2AQiKkLkRiduMkNkOkPk+d3A,d(g?qeuQkRkSiTitfufvfwfUixfyfzfAfzb-d.dBfCfDf/d)gEfFfNoAc@qSkTkUkVkOoPoQoGfHfVi4ARoSo*g+g,g-gToUoVoWoXoWiBc.g/g:d;d:gWkIfJfKfLf^cMfXkNfOfCc_c`c{c=dDcEcAbFcGcHcYoIc[qYkZk0k1k5AZo0o1o2oPfQfXifu6A3o4o7 %b'bJc|c}c~cad_ bdcd?dRfSf@dTfUf5oKc2k3k;g=g4k]qYiZi0i6oVfWf1i^q2i3i7oLc5k6k7k8k8o9o!oXfYf4i#o$o5i?gBb9kgu@g_q[g]g^g`q6i7i8i9iddhuedZf%o{q!i#i'omPnPfdgdXc[diuju(o!kMc|qoP7A#k8A$k%k'k9A)o*o+o,o0f1f$i}q~qpPkuluqP!Amu-o.o/o(kNcarrPsP)k#A*k+k,k$A:o;o=o?o2f3f%ibr%Anu@o[o]o-kOccrtP'A.k(A/k:k;k)A^o_o`o{o4f5f'idr*Aou|o}o~o=kPceruP+A?k,A@k[k]k-Aapbpcpdp6f7f(ifr.Apuepfpgp^kQcgrvP/A_k:A`k{k|k;Ahpipjpkp8f9f)ihr=Aqulpmpnp}kRcirwP?A~k@Aalblcl[Aopppqprp!f#f*ijr]ArusptpupdlSckrxPyPel^Aflglhl_Avpwpxpyp$f%f+isutu`AuuzpApBpilTclrzPAPjl{Aklllml|ACpDpEpFp'f(f,ivuwu}AxuGpHpBPCPDPEPFPGPHPIPJP`3KPLPMPNPOPPPQPRPSPTP{3|3UPVPWP}3XPYPZP0P1P2P3P4P5P6P7P8P9P!P#P$P%P'P(P)P~3*P+P,Pa4b4-P.P/P:Pc4;Pd4=Pe4?PwM@P[P]Pf4g4^Ph4_P`P(0{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQWri4qQrQsQtQLuMuNuOuPuQuRuSuTuUuVuWuXuYuZu0u1u2u3u4u5u6u7u8u9u!u#u$u%u'u(u)u*u+u,u-u.u/uuQvQwQ:u;u=uxQj4yQzQAQBQCQDQEQFQGQHQIQJQKQLQMQNQOQPQQQRQSQTQUQVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Q,Q-Q.Q/Q:Q;Q=Q?Qk4l4@Q[Qm4]Qn4^Q_Q`Q{Q|Q}Q~Qo4aRbRp4cRdReRq4fRgRr4hR)fXr*f+fYr,f-f.f/fZr0r:f1r2r;f3r=f?f4r@f[f5r]f6r^f_f`f{f7r|f8r9r}f!r#r~fagbgcgs4iRjRkRlRmRnRt4oRu4pRv4w4x4qRy4z4A4B4rRsRtRuRvRwRC4D4xRyRE4zRARBRF4CRG4H4DR
129cdef CUresult cuCtxGetCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
130 return _driver._cuCtxGetCurrent(pctx) 2a %sXRYRZR0R1R2R3R4R5R6R7R8R9R!R#R$R%R'R(R)R*R+R,R-R.R/R:R;R=R?R@R[R]R^R_R`R{R|R}R~RaSbScS~CaDbDcDdD}xeDfDgDhDiDjDkDlDmDnDoDpDqDrDsDtDdSuDvDwDxDyDsvzDADeSfSBDCDDDEDFD9 GD! HD# ID- JD+bKD,bLD-bMDVcNDgSODPDQDRDSDTDUDVDWDXDYDZD0D1DhStvuv2D3DiS*l4D+l5D6Dde7DOh8DPh9DQh!DRh#D,l$D-l%D'D(D)DjSvvwv*D+DkS=l,D?l-D.Dge/DSh:DTh;DUh=DVh?D@l@D[l[D]D^D_D`D{D|D}D~DaEbEcEdEeEfEgEhEiExvyvjEkElEemmEfmnEoEjepEWhqEXhrEYhsEZhtEgmuEhmvEwExEyEzEzvAvAEBECEmmDEnmEEFEmeGE0hHE1hIE2hJE3hKEomLEpmMENEOEPEQEBvCvRESETEumUEvmVEWEpeXE4hYE5hZE6h0E7h1Ewm2Exm3E4E5E6E7EDvEv8E9E!ECm#EDm$E%Ese'E8h(E9h)E!h*E#h+EEm,EFm-E.E/E:E;E=E?E@E[E]E^E_E`ElS{E|E}E~EaFbF4lmSnSoSpSqS~xrSsStSuSvSwSxSySzS5lASBSCSDSESFSGSHSISWpJSXpKSYpLSZpMSHbNSIbOSJbPSKbQSRSSSTSUSVSWSXSYSZS0S1S2S3S4S5S6S7S8S9Saj!S#S$S%S'S(S)S*S+S,Sb -S.S{b/S:S;S=S?S@S[S]S^S_S`S{S|S}S~ScFdFeFfFgFaTbThFiFcTjFkFlFmFdTnFoFeTfTgThTiTjTkTlTmTnToTpTqTrTsTeBfB_gtT`guTvTwTxTyTzTATBTCTDTET)0gBhBiBjBkBlBmBnBoBpBqBrBsBtBuBvBwBxB*syBzBABBBCBDBEBFB+sGBHBIBJBKBLBMBNBOBPBQBRBSBTB,sUB-sVBWBXBYBZB0B1B2B3B4B5B6B7B8B9B!B#B$B%B'B(B)B*B+B,B-B.B/B:B;B=B?B@B[B]B^B_B.s`B{B|B}B~B/saCbCcCdCeCfCgChC:siCjCkClCmC;snCoCpCqCrCsCtCuC=svCwCxCyCzCACBCCCDCECFCGCHCICJCKCLC?sMC@sNCOCPC[sQCRCSCTCUCVCFTtMGTHTIT~A*0]sI4aBYc3 ZcJTWmKTLTMTNTOTPTQTRTSTTTUTVTWTXTYTZTHl0TpFqFrFX 1TY 2T}CsFtFuF3TvFwFxF4T5T6T7T8T9T!T#T$T%T'T(T)T*T+T,T-T.T/Txedc:T;T=T?T0c1c2c@T[T]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUogZm0mBtCtuMDtEtFtGtHtItJtKtLtMtNtOtPtQtRtStTtUtVtWtXtYtZt0t1t2tvM3t4t5t6t7t8t9t!t#t$t%t'tAUBUCUDUEUFUGUHUIUJUKULUMUNUOUPUQURUSUTUUUVUWUXUYUZU0U1U2U3U4U5U6U7U8U9U!U#U$U%U'U(U)U*U+U,U-U.U/U:U;U=U?U@U[U]U^U_U`U{U|U}U~UaVbVcVdVeV)t1m_hKefVgVhViVjVkVlVmV0bcbnVoVpVqVrVsVtVuVvVwVxVyVNhzVAVBVCVDVEVFVGVHVIVJVKVLVMVNVOVPVQVRVSVTVUVVVWVXVYVZV0V1V2V3V4V5V6V7V8V9V!V#V$V%V'V(V)V*V+V,V-V.V/V:V;V=V?V@V[V]V^V_V`V{V|V}V~VaWbWcWdWeWfWgWhWiWjWkWlWmWnWoWpWqWrWsWtWuWvWwWxWyWzWyFzFAF7qBFAWBWCFDFFvGvEFFFGFWnHFXnIFCWJFNeKF|hLFDWMFNFUrOFZnPFQFEWRFSFTFUF9qVFFWGWWFXFHvIvYFZF0F3n1FVr2FHW3FPe4F}h5FIW6F7F5n8F6n9F!FJvKv#F$Fzg%FAg'F(FSe)F~h*FBg+FCg,FLvMvUeNvOvKrLrPvQvRvNdSvOdTv-FUv.F2bVv!cWv/FXvPdYvQdZv0v1v:F/ ;F: =F; ?F= @Fci[Fqb]FEg^F~i2vFg3vGg_Fdi`F7n{F8n|F#c}FRd~FHgaG#qbG9ncG!ndGeGfGgG$qhGiG4v5vjGkGlG%nmG'nnGJWoGKWXepGeiqGLWrG)nsG*ntGuGvGwG+nxGMWyGzG6v7vAGBGCG:jDG;jEGNWFGOWTdGGIgHGPWIGJG?jKG@jLGMGNG8v9vOGPGZeQG0eRGSG1eTGJgUG2eVG3eWG!v#v$v-n%vXG'v(v)v*v+v,v{j-v|j.vYG/vZGXd:vKg;v0G=v~j?vak@v[v]v4e^v5e_v6e`v7e{v|v8e}v9e~v!eaw#ebw1Gcwdw2G%e3G'e4G0d5GLg6G(e7G)e8G9G!G(q#G$Gewfw%G'G;n(G=n)G*G+e+Gri,G-G?n.G@n/GMg:GNg;GOg=GPg?G[n@G]n[G^n]G_n^G`n_G`G{GQg|G}Ggwhw~GaHbH-ecH.edHeH%cfH:egHhH;eiH=ejHkHiwjwlHmHocnHpcoHtbpHqcqHrcrHscsHtHuH)qvHwHkwlwxHyHzH}nAH~nBHQWCH@eDHtiEHRWFHboGHcoHH6 IH6bmw7bnwucJH*cKH+cLH,cMH-cNH? OH.cow/cpw4dPH[eQH]eRH5dSH^eTH_eUHVHWHuiXHYHqwrwZH0H1HUg2HVg3HSW4H6d5HWg6H7HXg8HYg9H!H#H$Hswtw%H'Hio(Hjo)H*H~e+Hxi,Hko-Hlo.Huwvwwwpkxw/HywzwMrNrAwBwCwAiDwBiEw:HFw;H;cGwafHw=HIwDiJwEiKwmo?H@H[H]H.q^HTWUW_H`HLwMw{H|H}Hpo~HqoaIVWbIcfcIFidIWWeIfIsogItohIiINwOwjIkI5glI6gmInIffoIGipI7gqI8grIPwQwhfRwSwOrPrTwUwVw#dWw$dXwsIYwtI!bZw@c0wuI1w%d2w'd3w4w5wvI@ wI[ xI] yI^ zIKiAIxbBI9gCI!g6w#g7w$gDILiEIuoFIvoGI[cHI(dII%gJI:qKIwoLIxoMINIOIPI;qQIRI8w9wSITIUIAoVIBoWIXWXIYWkfYIMiZIZW0IDo1IEo2I3I4I5I=q6I0W7I8I!w#w9I!I#IHo$IIo%I1W'I2Wmf(INi)I3W*I+IKo,ILo-I.I/I$w%w:I;Iof=Ipf?I@Iqf[I'g]Irf^Isf_I'w(w)wMo*w`I+w,w-w.w/w:wNk;wOk=w{I?w|I,d@w(g[w}I]wQk^wRk_w`w{wtf|wuf}wvf~wwfaxbxxfcxyfdxzfexAffx~IgxhxaJCfbJDfcJ/ddJ)geJEffJFfgJhJiJ@qjJkJixjxlJmJPonJQooJpJHfqJVirJsJRotJSouJ*gvJ+gwJ,gxJ-gyJTozJUoAJVoBJWoCJXoDJEJFJ.gGJHJkxlxIJJJKJJfLJKfMJNJ^cOJMfPJQJNfRJOfSJTJmxnxUJVJDcWJEcXJAbYJFcZJGc0JHc1J2J3J[q4J5Joxpx6J7J8J0o9J1o!J4W#JQf$JXi%J5W'J3o(J4o)J7 *J%bqx'brxJc+J|c,J}c-J~c.Jad/J_ :Jbdsxcdtx?d;JRf=JSf?J@d@JTf[JUf]J^J_J2k`J{Juxvx|J}J~JZiaK0ibK6WcKWfdK1ieKfK2igK3ihKiKjKkKwxxxlKmK9onK!ooKpKYfqK4irK#osK$otKyxzxAx9kBxuKCxDxQrRrExFxGx7iHx8iIxvKJxwKedKxZfLxxKMx!iNx#iOx'oyK7W8W9W!WzKAKBK|qCK#W$WDKEKPxQxFKGKHK*oIK+oJK%WKK1fLK$iMK'W(W)W*W+W,WNKOK-oPK.oQKRKSKTKarUK-W.WVKWKRxSxXKYKZK;o0K=o1K/W2K3f3K%i4K:W5K6K@o7K[o8K9K!K#Kcr$K;W=W%K'KTxUx(K)K*K_o+K`o,K?W-K5f.K'i/K@W:K;K|o=K}o?K@K[K]Ker^K[W]W_K`KVxWx{K|K}Kbp~KcpaL^WbL7fcL(idL_WeLfLepgLfphLiLjLkLgrlL`W{WmLnLXxYxoLpLqLiprLjpsL|WtL9fuL)ivL}WwLxLlpyLmpzLALBLCLirDL~WaXELFLZx0xGLHLILppJLqpKLbXLL#fML*iNLcXOLPLspQLtpRLSLTLULkrVLdXeXWLXL1x2xYLZL0Lwp1Lxp2LfX3L%f4L+i5LgXhX6L7Lzp8LAp9L!L#L$Llr%LiXjX'L(L3x4x)L*L+LDp,LEp-LkX.L(f/L,i:LlXmX;L=LGp?LHp@LnXoXyupXqXrXsXtXuXvXwXxXyXzXAXBXCXDXEXFXGXHXIXJXKXLXMXNXOXPXQXRXSXTXUXVXWXXXYXZX0X1X2X3X+0zuAunj4X5X6X7X8X9X!X#X$X%X'X(X)X*X,0BuCuDuEuFu+XGuHuIuJuKu,X-X.X/XwM:X;X=X?X@X[X]X^X_X`X{X|X}X~XaYbYcYdY$reYfYgYhYiYjYkYlYmYnYoYpYqYrYsYtYuYvYwYxYyYzYAYBYCYDYEYFYGYHYIYJYKYLYMYNYOYPYQYRYSYTYUYVYWYXYYYZY0Y1Y2Y3Y4Y5Y6Y7Y8Y9Y!Y#Y$Y%Y'Y(Y)Y*Y+Y,Y-Y.Y/Y:Y;Y=Y?Y@Y[Y]Y^Y_Y`Y{Y|Y}Y~YaZbZcZdZeZfZgZhZiZjZkZlZmZnZoZpZqZrZsZtZuZvZwZxZyZzZAZBZCZDZEZFZGZHZIZJZKZLZMZNZOZPZQZRZSZTZUZVZWZXZYZZZ0Z1Z2Z3Z4Z5Z6Z)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}f~fagbgcg7Z8Z9Z!Z#Z$Z%Z'Z(Z)Z*Z+Z,Z-Z.Z/Z:Z;Z=Z?Z@Z[Z]Z^Z_Z`Z{Z|Z}Z~Za0b0c0d0e0f0g0h0
133cdef CUresult cuCtxGetDevice(CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil:
134 return _driver._cuCtxGetDevice(device) 2a %sbjObPbggU (b{ cjV Ucdj8 4 ay, Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L bBcBnrJ4Js`udB{u9loj!lpj#l$lorpdhdidjd]d5 ]bqdrdDbEbFb*bGb9 ! # - +b,b-bVcprqrrrsrtrur/inl%l'l|bqjbecerjxddeOhPhQhRh.l/l}bsjeefetjydgeShThUhVh]luj^lvj_l`l{lwj|lxj}l~lambm~byjheiezjzdjeWhXhYhZhimjmacAjkeleBjAdme0h1h2h3hqmrmbcQpneoeCjBdpe4h5h6h7hymzmccDjqereEjCdse8h9h!h#hGmFjHmGjImJmKmHjLmIjMmNmOmJjPmKjQmRmolvr^dkdFRGRHRK4IRJRHbIbJbKb^b_b.bIh_dejQbRb`dfjM P wrdg0 | } /b`bQ N A B C b y $ z x D abE F R S T L4G 1 2 Lb:b;bld=bW Jq8lM4KqLqNqPqQqRqxrTmLj(sUmMj%rVm'rNj)sSqTqUqVqWqXqYqZq0q`i5x6x7x8x9x!xOjyr#x$x%x'x(x)x*x+x,x-xQj.x/x:x;x=xRj?x@x[x]xbycydyeyfygyeBfB_g`gxMhy)0gBhBiBjBkBlBmBnBoBpBqBrBsBtBuBvBwBxB*syBzBABBBCBDBEBFB+sGBHBIBJBKBLBMBNBOBPBQBRBSBTB,sUB-sVBWBXBYBZB0B1B2B3B4B5B6B7B8B9B!B#B$B%B'B(B)B*B+B,B-B.B/B:B;B=B?B@B[B]B^B_B.s`B{B|B}B~B/saCbCcCdCeCfCgChC:siCjCkClCmC;snCoCpCqCrCsCtCuC=svCwCxCyCzCACBCCCDCECFCGCHCICJCKCLC?sMC@sNCOCPC[sQCRCSCTCUCVCtM~A*0]saBYc3 ZcyMWmzMIlJlKlLlMlNl~ OlPlQlRlSlgjJhWcNb|ixedcN4O4hjihjhkh0c1clhmhnhoh2cphqhrhshfgthuhvhwhxhyhzhAhBhChDhEhFhGhHhP4^s_s`sQ4{s|s}s~satbtctWCdtetftgthtitjtktltmtntotptqtrtstttutvtwtxtytztXCAtog}d~dZmi0SrTr0mj0k0l0m0n0o0p0q0BtCtr0uMDts0EtFtt0u0Gtv0w0x0y0Htz0ItJtA0B0C0KtD0E0LtMtF0NtG0H0OtPtQtI0J0K0RtL0M0N0O0StP0Q0TtUtR0S0VtWtXtYtT0U0V0Zt0tW01tX02tvM3tY04tZ05t00106t7t8t209t!t30#t4050$t6070%t8090!0#0't$0%0Gl]i^iYbR4pl3c|uql}u(h)h*h~umb_iDdrlS4+hyeEd4c,hze-hAe.hqg/hBeFdec:hCe;hYC5cZCrg0Csg1Ctg2Cug3C6c4Cvg5C=hDeGdfc?hEe@hFe[hGe1jHeHdgc]hIewgxg^hJe7cId)t|x1m_h{gKeslZbhcLe2m`h{hLRTlUlmd0bcbMRnd6CNR3m-04miy5mzr6m.07m/08mO 9mNhArBrCrDrErFrGrHrIrJr!m#m$m%m*t+t,t'0-t.t/t:t;t7C'm8C(m9C)m!C*m#C+m$C,mav-mbv.mcv/mdv:mev;mfv=mgv?mhv@miv[mjv]mkv^mlv_mmv`mnv{mov|mpv}mqv~mrvanT4bnU4cn%Cdn'Cen(Cfn)Cgn*Chn+Cin,Cjn-Ckn.Cln/Cmn:Cnn;Con=Cpn?Cqn@Crn[Csn]Ctn^Cun_Cvn`Cwn{CxnV4yn:0zn;0An=0Bn?0Cn@0Dn[0En]0Fn^0Gn_0Hn`0In{0Jn|0Kn}0Ln~0Mna1Nnb1OnPnUnic4j7jYnMeNe|h8q0n1njc!j%j4nOePe}h!q1bQeRe'jygzgAgJdSe~hBgCgTe* KdLdVenb2b!cDgobpb3b/ : ; = ciqbEgGg#cRdHg#nkc*j-j(nWeXeei%q.j4bgiji=jSdTdIg,n[jrbUdVdkiYeZe0e$c1eJg2e3e]j5bmini}jWdXdKg.nsbYdZd$e%e'e0dLg(e)e/nlcbkek*e+erisimcQgRg1d2dSgfk,e-e.e/e%c:egk;e=enc'c(c)c3docpctbqcrcsc{ntchkkkao?e@eti*q6 6b7buc*c+c,c-c? .c/c4d[e]e5d^e_elkvcuivi`e{ewidoTgUgVgeo|e6dWgfoXgYggowcmkok}e~exiyiub0g3gCi:c;cafqknoxcskvkrobfcfFi/q8bdfefwk4g5g6g7dffGi7g8ggf+ 8d9dif9b!b@cIivbwb#b@ [ ] ^ Kixb9g$g[c(d%gyoyczkCkCojfkfMiauFozcEkHkJolfmfNibuIkyb)d*dOinfofpf]cqf'grfsfJk$bQiRiPk+d,d(g?qzb-d.dBfCfDf/d)gEfFfNoAcSkVkGfHfViWiBc.g/g:d;d:gWkIfJfKfLf^cMfXkNfOfCc_c`c{c=dDcEcAbFcGcHcYoIcYk1k2oPfQfXifu7 %b'bJc|c}c~cad_ bdcd?dRfSf@dTfUf5oKc2k3k;g=g4k]qYiZi0i6oVfWf1i^q2i3i7oLc5k8kXfYf4i5iBb@g^g9iddedZf%oiuju(oMc#k'k,o0f1f$i}q~qkulu/oNc)k,k?o2f3f%ibr]oOc.k;k{o4f5f'idr~oPc?k]kdp6f7f(ifrgpQc_k|kkp8f9f)ihrnpRc~kclrp!f#f*ijrupScelhlyp$f%f+isutuBpTcjlmlFp'f(f,ivuwuORPRyuQRRRSRTR+0zuAunj,0BuCuDuEuFuURGuHuIuJuKuW4wMAM(0X4jykylymynyoy$rpyqyrysytyuyvywyxyVlyyWr(rzyKhAyLuMuNuOuPuQuRuSuTuUuVuWuXuYuZu0u1u2u3u4u5u6u7u8u9u!u#u$u%u'u(u)u*u+u,u-u.u/u:u;u=u)rBMCMDMEMFMGMZ HMod0pijjjIM*rJM+rhgtlulvlwlxlylKMzlAlBlClDl,r-rElLMMM.r|g/r}g:rNMOMPMQMRMSMLhY4Z404142434445464748494!4#4$4%4'4(4)4*4+4,4-4.4)fXr*f+fYr,f-f.f/fZr0r:f1r2r;f3r=f?f4r@f[f5r]f6r^f_f`f{f7r|f8r9r}f!r#r~fagbgcg/4:4;4
137cdef CUresult cuCtxGetFlags(unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
138 return _driver._cuCtxGetFlags(flags)
141cdef CUresult cuCtxSetFlags(unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
142 return _driver._cuCtxSetFlags(flags)
145cdef CUresult cuCtxGetId(CUcontext ctx, unsigned long long* ctxId) except ?CUDA_ERROR_NOT_FOUND nogil:
146 return _driver._cuCtxGetId(ctx, ctxId)
149cdef CUresult cuCtxSynchronize() except ?CUDA_ERROR_NOT_FOUND nogil:
150 return _driver._cuCtxSynchronize()
153cdef CUresult cuCtxSetLimit(CUlimit limit, size_t value) except ?CUDA_ERROR_NOT_FOUND nogil:
154 return _driver._cuCtxSetLimit(limit, value)
157cdef CUresult cuCtxGetLimit(size_t* pvalue, CUlimit limit) except ?CUDA_ERROR_NOT_FOUND nogil:
158 return _driver._cuCtxGetLimit(pvalue, limit)
161cdef CUresult cuCtxGetCacheConfig(CUfunc_cache* pconfig) except ?CUDA_ERROR_NOT_FOUND nogil:
162 return _driver._cuCtxGetCacheConfig(pconfig)
165cdef CUresult cuCtxSetCacheConfig(CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
166 return _driver._cuCtxSetCacheConfig(config)
169cdef CUresult cuCtxGetApiVersion(CUcontext ctx, unsigned int* version) except ?CUDA_ERROR_NOT_FOUND nogil:
170 return _driver._cuCtxGetApiVersion(ctx, version)
173cdef CUresult cuCtxGetStreamPriorityRange(int* leastPriority, int* greatestPriority) except ?CUDA_ERROR_NOT_FOUND nogil:
174 return _driver._cuCtxGetStreamPriorityRange(leastPriority, greatestPriority) 2bjObPbggU (b{ cjV Ucdj8 4 ay, Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L pdhdidjd]d5 ]bqdrdDbEbFb*bGb9 ! # - +b,b-bVckd^b_bQbRbM P 0 | } `bQ N A B C b ?b@b[bsdtdudy $ z x D abE F R S T SbTbUb% ' ( G 1 2 Lb:b;bld=bW igaeWlXlvdYlZl%r'rjgkg1p2p3p4p5p`i) ` KpLpMpdbNp-iOpPp0lTMUMng.iebfb. VbWbXbgbhbibjbkblbbycydyeyfygyhyYc3 ZcIlJlKlLlMlNl~ OlPlQlRlSlgjJhWc~gUpahbhSjchdheh{ifhghhhFlByMbX Y c1VMkjNb|ixedchj}d~d;r=r6p?r7p@r[r8p9p]r^r_r!p`r#p$p%p'p(p)p*p+p,p{r-p.p/p:p|r;p=p}r~rasbs?pcs@pdses[p]pfsgshs^pis_p`p{p|p}p~paqbqcqjsdqeqfqgqkshqiqlsmsnsosjqpskqqsrslqmqsstsusnqvsoqpqqqrqsqtquqvqwqwsxqyqzqAqxsBqCqyszsYbmb_hZbTlUlO }i?t@t[t'qyiZgubpk|t0g+q1g2g3g,qziAiBiCi:c}t;cafqk-qDiEi~tcu5i?gBb9kgu@g_q[g]g^g`q6i7i8i9iddhuedZf%o{q!i#iXc[dmunuoupuquruuuxujykylymynyoy$rpyqyrysytyuyvywyxyVlyyWr(rzyKhAyZ od0pijjjhgwd
177cdef CUresult cuCtxResetPersistingL2Cache() except ?CUDA_ERROR_NOT_FOUND nogil:
178 return _driver._cuCtxResetPersistingL2Cache()
181cdef CUresult cuCtxGetExecAffinity(CUexecAffinityParam* pExecAffinity, CUexecAffinityType type) except ?CUDA_ERROR_NOT_FOUND nogil:
182 return _driver._cuCtxGetExecAffinity(pExecAffinity, type)
185cdef CUresult cuCtxRecordEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
186 return _driver._cuCtxRecordEvent(hCtx, hEvent)
189cdef CUresult cuCtxWaitEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
190 return _driver._cuCtxWaitEvent(hCtx, hEvent)
193cdef CUresult cuCtxAttach(CUcontext* pctx, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
194 return _driver._cuCtxAttach(pctx, flags)
197cdef CUresult cuCtxDetach(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
198 return _driver._cuCtxDetach(ctx)
201cdef CUresult cuCtxGetSharedMemConfig(CUsharedconfig* pConfig) except ?CUDA_ERROR_NOT_FOUND nogil:
202 return _driver._cuCtxGetSharedMemConfig(pConfig)
205cdef CUresult cuCtxSetSharedMemConfig(CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
206 return _driver._cuCtxSetSharedMemConfig(config)
209cdef CUresult cuModuleLoad(CUmodule* module, const char* fname) except ?CUDA_ERROR_NOT_FOUND nogil:
210 return _driver._cuModuleLoad(module, fname)
213cdef CUresult cuModuleLoadData(CUmodule* module, const void* image) except ?CUDA_ERROR_NOT_FOUND nogil:
214 return _driver._cuModuleLoadData(module, image) 2{d|d:i;i=ieg?i@i
217cdef CUresult cuModuleLoadDataEx(CUmodule* module, const void* image, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
218 return _driver._cuModuleLoadDataEx(module, image, numOptions, options, optionValues) 2=4
221cdef CUresult cuModuleLoadFatBinary(CUmodule* module, const void* fatCubin) except ?CUDA_ERROR_NOT_FOUND nogil:
222 return _driver._cuModuleLoadFatBinary(module, fatCubin)
225cdef CUresult cuModuleUnload(CUmodule hmod) except ?CUDA_ERROR_NOT_FOUND nogil:
226 return _driver._cuModuleUnload(hmod) 2{d|d:i;i=ieg?i@i
229cdef CUresult cuModuleGetLoadingMode(CUmoduleLoadingMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
230 return _driver._cuModuleGetLoadingMode(mode)
233cdef CUresult cuModuleGetFunction(CUfunction* hfunc, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
234 return _driver._cuModuleGetFunction(hfunc, hmod, name) 2{d|d:i;i=ieg?i@i
237cdef CUresult cuModuleGetFunctionCount(unsigned int* count, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
238 return _driver._cuModuleGetFunctionCount(count, mod)
241cdef CUresult cuModuleEnumerateFunctions(CUfunction* functions, unsigned int numFunctions, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
242 return _driver._cuModuleEnumerateFunctions(functions, numFunctions, mod)
245cdef CUresult cuModuleGetGlobal(CUdeviceptr* dptr, size_t* bytes, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
246 return _driver._cuModuleGetGlobal_v2(dptr, bytes, hmod, name) 2eg
249cdef CUresult cuLinkCreate(unsigned int numOptions, CUjit_option* options, void** optionValues, CUlinkState* stateOut) except ?CUDA_ERROR_NOT_FOUND nogil:
250 return _driver._cuLinkCreate_v2(numOptions, options, optionValues, stateOut)
253cdef CUresult cuLinkAddData(CUlinkState state, CUjitInputType type, void* data, size_t size, const char* name, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
254 return _driver._cuLinkAddData_v2(state, type, data, size, name, numOptions, options, optionValues)
257cdef CUresult cuLinkAddFile(CUlinkState state, CUjitInputType type, const char* path, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
258 return _driver._cuLinkAddFile_v2(state, type, path, numOptions, options, optionValues)
261cdef CUresult cuLinkComplete(CUlinkState state, void** cubinOut, size_t* sizeOut) except ?CUDA_ERROR_NOT_FOUND nogil:
262 return _driver._cuLinkComplete(state, cubinOut, sizeOut)
265cdef CUresult cuLinkDestroy(CUlinkState state) except ?CUDA_ERROR_NOT_FOUND nogil:
266 return _driver._cuLinkDestroy(state)
269cdef CUresult cuModuleGetTexRef(CUtexref* pTexRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
270 return _driver._cuModuleGetTexRef(pTexRef, hmod, name)
273cdef CUresult cuModuleGetSurfRef(CUsurfref* pSurfRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
274 return _driver._cuModuleGetSurfRef(pSurfRef, hmod, name)
277cdef 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:
278 return _driver._cuLibraryLoadData(library, code, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2U (b{ V Uc8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L 5 DbEbFb*bGb/inl|bxd}byd~bzdacAdbcBdccCd^dHbIbJbKb.bM P wrdg0 | } /bQ N A B C b y $ z x D abE F R S T G 1 2 Lb:b;bld=bW ) ` 3 ~ WcweXmYmNbdchjihjhkh0c1clhmhnhoh2cphqhrhshfgthuhvhwhxhyhzhAhBhChDhEhFhGhHh3m4miy5mzr6m7m8mO 9mNhArBrCrDrErFrGrHrIrJr!m#m$md1%me1?4'm(m)m*m+m,m-m.m/m:m;m=m?m@m[m]m^m_m`m{m|m}m~manbncndnenfngnhninjnknlnmnnnonpnqnrnsntnunvnwnxnynznAnBnCnDnEnFnGnHnInJnKnLnMnNnOnPnicYnMe8q0njc4nOe!q1bJd* VenbDgobpb3b/ : ; = qb#ckc(nWe%q4b=jSd,nrb$c5b}jWd.nsblc*esimcQgRg1d2dSgfk,e-e.e/e%c:egk;e=enc'c(c)c3docpctbqcrcsctcao?e*q6 ? lkvcuivi`e{ewidoTgUgVgeo|e6dWgfoXgYgwc}eubCi:cqkxcrobf/q8b7d+ if9bvbwb#b@ [ ] ^ xb[cycCojfzcJolfyb]c$bPk+dzbAcGfWiBc.g/g:d;d:gWkIfJfKfLf^cMfXkNfOfCc_c`c{c=dDcEcAbFcGcHcIc2oPf7 _ Kc6oVfLcXfBb9iddMc,o0f}q~qNc?o2fbrOc{o4fdrPcdp6ffrQckp8fhrRcrp!fjrScyp$fTcFp'fnjAM
281cdef 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:
282 return _driver._cuLibraryLoadFromFile(library, fileName, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2f1g1h1i1
285cdef CUresult cuLibraryUnload(CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
286 return _driver._cuLibraryUnload(library)
289cdef CUresult cuLibraryGetKernel(CUkernel* pKernel, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
290 return _driver._cuLibraryGetKernel(pKernel, library, name) 2U (b{ V Uc8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L 5 DbEbFb*bGb/inl|bxd}byd~bzdacAdbcBdccCd^dHbIbJbKb.bM P wrdg0 | } /bQ N A B C b y $ z x D abE F R S T G 1 2 Lb:b;bld=bW ) ` 3 ~ WcweXmYmNbdchjihjhkh0c1clhmhnhoh2cphqhrhshfgthuhvhwhxhyhzhAhBhChDhEhFhGhHh3m4miy5mzr6m7m8mO 9mNhArBrCrDrErFrGrHrIrJr!mf1#mg1$md1%mh1i1e1'm(m)m*m+m,m-m.m/m:m;m=m?m@m[m]m^m_m`m{m|m}m~manbncndnenfngnhninjnknlnmnnnonpnqnrnsntnunvnwnxnynznAnBnCnDnEnFnGnHnInJnKnLnMnNnOnPnicYnMe0njc4nOe1bJd* Venbobpb3b/ : ; = qb#ckc(nWe4b=jSdrb$c5b}jWdsblc*esimcQgRg1d2dSgfk,e-e.e/e%c:egk;e=enc'c(c)c3docpctbqcrcsctcao?e6 ? vceo|ewc}eubCi:cxcrobf8b7d+ if9bvbwb#b@ [ ] ^ xb[cycCojfzcJolfyb]c$bPk+dzbAcGfWiBc.g/g:d;d:gWkIfJfKfLf^cMfXkNfOfCc_c`c{c=dDcEcAbFcGcHcIc2oPf7 _ Kc6oVfLcXfBb9iddMc,o0fNc?o2fOc{o4fPcdp6fQckp8fRcrp!fScyp$fTcFp'fnjAM
293cdef CUresult cuLibraryGetKernelCount(unsigned int* count, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
294 return _driver._cuLibraryGetKernelCount(count, lib)
297cdef CUresult cuLibraryEnumerateKernels(CUkernel* kernels, unsigned int numKernels, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
298 return _driver._cuLibraryEnumerateKernels(kernels, numKernels, lib)
301cdef CUresult cuLibraryGetModule(CUmodule* pMod, CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
302 return _driver._cuLibraryGetModule(pMod, library)
305cdef CUresult cuKernelGetFunction(CUfunction* pFunc, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
306 return _driver._cuKernelGetFunction(pFunc, kernel)
309cdef CUresult cuKernelGetLibrary(CUlibrary* pLib, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
310 return _driver._cuKernelGetLibrary(pLib, kernel)
313cdef CUresult cuLibraryGetGlobal(CUdeviceptr* dptr, size_t* bytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
314 return _driver._cuLibraryGetGlobal(dptr, bytes, library, name)
317cdef CUresult cuLibraryGetManaged(CUdeviceptr* dptr, size_t* bytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
318 return _driver._cuLibraryGetManaged(dptr, bytes, library, name)
321cdef CUresult cuLibraryGetUnifiedFunction(void** fptr, CUlibrary library, const char* symbol) except ?CUDA_ERROR_NOT_FOUND nogil:
322 return _driver._cuLibraryGetUnifiedFunction(fptr, library, symbol)
325cdef CUresult cuKernelGetAttribute(int* pi, CUfunction_attribute attrib, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
326 return _driver._cuKernelGetAttribute(pi, attrib, kernel, dev) 2wrdg0 -0iyzr.0/0avbvcvdvevfvgvhvivjvkvlvmvnvovpvqvrv:0;0=0?0@0[0]0^0_0`0{0|0}0~0a1b1
329cdef CUresult cuKernelSetAttribute(CUfunction_attribute attrib, int val, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
330 return _driver._cuKernelSetAttribute(attrib, val, kernel, dev)
333cdef CUresult cuKernelSetCacheConfig(CUkernel kernel, CUfunc_cache config, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
334 return _driver._cuKernelSetCacheConfig(kernel, config, dev)
337cdef CUresult cuKernelGetName(const char** name, CUkernel hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
338 return _driver._cuKernelGetName(name, hfunc) 2@4
341cdef CUresult cuKernelGetParamInfo(CUkernel kernel, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil:
342 return _driver._cuKernelGetParamInfo(kernel, paramIndex, paramOffset, paramSize) 2O NhArBrCrDrErFrGrHrIrJr[4
345cdef CUresult cuMemGetInfo(size_t* free, size_t* total) except ?CUDA_ERROR_NOT_FOUND nogil:
346 return _driver._cuMemGetInfo_v2(free, total)
349cdef CUresult cuMemAlloc(CUdeviceptr* dptr, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil:
350 return _driver._cuMemAlloc_v2(dptr, bytesize) 2`iCyj1bbAsk1Bsl1m1n1o1p11lDqCsDsEqWMXMYMq1{d|dog}d~dZm0m;r=r6p?r7p@r[r8p9p]r^r_r!p`r#p$p%p'p(p)p*p+p,p{r-p.p/p:p|r;p=p}r~rGl|x1m_hTlUl
353cdef CUresult cuMemAllocPitch(CUdeviceptr* dptr, size_t* pPitch, size_t WidthInBytes, size_t Height, unsigned int ElementSizeBytes) except ?CUDA_ERROR_NOT_FOUND nogil:
354 return _driver._cuMemAllocPitch_v2(dptr, pPitch, WidthInBytes, Height, ElementSizeBytes)
357cdef CUresult cuMemFree(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
358 return _driver._cuMemFree_v2(dptr) 2y $ z x D abE F R S T cFdFeFfFgFxrhFjFlFEsnFoF`idbmgveebfb. WbXbgbhbibjbkblbRpCyFsj1bbAsk1Bsl1m1n1o1p11lDqCsDsEqWMXMYMNb|ixeq1{d|dog}d~dZmTr0m5q^x;r=r6p?r7p@r[r8p9p]r^r_r!p`r#p$p%p'p(p)p*p+p,p{r-p.p/p:p|r;p=p}r~rnsosjqpskqqsrslqmqsstsusnqvsoqpqqqrqsqtquqvqwqwsxqyqzqAqxsBqCqyszsGlpl|x1m_hTlUl
361cdef CUresult cuMemGetAddressRange(CUdeviceptr* pbase, size_t* psize, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
362 return _driver._cuMemGetAddressRange_v2(pbase, psize, dptr)
365cdef CUresult cuMemAllocHost(void** pp, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil:
366 return _driver._cuMemAllocHost_v2(pp, bytesize) 2U 4 c d e f g h i j k l m n o p q r H s t u v w I J K L Q N A B C b {bG 1 2 ) ` 3 ~ MbX Y Nbihjhkh0c1clhmhnhoh2cphqhrhshfgthuhvhwhxhyhzhAhBhChDhEhFhGhHhog}d~dSr_x`xasbs?pcs@pdses[p]pfsgshs^pis_p`p{p|p}p~paqbqcqjsdqeqfqgqkshqiqlsmsGlO
369cdef CUresult cuMemFreeHost(void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
370 return _driver._cuMemFreeHost(p) 2U 4 c d e f g h i j k l m n o p q r H s t u v w I J K L Q N A B C b {bG 1 2 dbr1s13 ~ MbX Y Nbihjhkh0c1clhmhnhoh2cphqhrhshfgthuhvhwhxhyhzhAhBhChDhEhFhGhHhog}d~dSr_x`xasbs?pcs@pdses[p]pfsgshs^pis_p`p{p|p}p~paqbqcqjsdqeqfqgqkshqiqlsmsGlO
373cdef CUresult cuMemHostAlloc(void** pp, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
374 return _driver._cuMemHostAlloc(pp, bytesize, Flags) 2r1s1
377cdef CUresult cuMemHostGetDevicePointer(CUdeviceptr* pdptr, void* p, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
378 return _driver._cuMemHostGetDevicePointer_v2(pdptr, p, Flags)
381cdef CUresult cuMemHostGetFlags(unsigned int* pFlags, void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
382 return _driver._cuMemHostGetFlags(pFlags, p)
385cdef CUresult cuMemAllocManaged(CUdeviceptr* dptr, size_t bytesize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
386 return _driver._cuMemAllocManaged(dptr, bytesize, flags) 2y $ z x D abE F R S T KqLqNqPqQqxrTmUmVmEsSqTq) ` ng.iebfb. VbWbXbgbhbibjbkblbRpFsNb|ixeog}d~dTr5q^xnsosjqpskqqsrslqmqsstsusnqvsoqpqqqrqsqtquqvqwqwsxqyqzqAqxsBqCqyszsGlpl
389cdef CUresult cuDeviceRegisterAsyncNotification(CUdevice device, CUasyncCallback callbackFunc, void* userData, CUasyncCallbackHandle* callback) except ?CUDA_ERROR_NOT_FOUND nogil:
390 return _driver._cuDeviceRegisterAsyncNotification(device, callbackFunc, userData, callback)
393cdef CUresult cuDeviceUnregisterAsyncNotification(CUdevice device, CUasyncCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
394 return _driver._cuDeviceUnregisterAsyncNotification(device, callback)
397cdef CUresult cuDeviceGetByPCIBusId(CUdevice* dev, const char* pciBusId) except ?CUDA_ERROR_NOT_FOUND nogil:
398 return _driver._cuDeviceGetByPCIBusId(dev, pciBusId)
401cdef CUresult cuDeviceGetPCIBusId(char* pciBusId, int len, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
402 return _driver._cuDeviceGetPCIBusId(pciBusId, len, dev)
405cdef CUresult cuIpcGetEventHandle(CUipcEventHandle* pHandle, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
406 return _driver._cuIpcGetEventHandle(pHandle, event) 2) ` KpLpMpdbNp-iOpPp0l}iXc[d
409cdef CUresult cuIpcOpenEventHandle(CUevent* phEvent, CUipcEventHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
410 return _driver._cuIpcOpenEventHandle(phEvent, handle)
413cdef CUresult cuIpcGetMemHandle(CUipcMemHandle* pHandle, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
414 return _driver._cuIpcGetMemHandle(pHandle, dptr)
417cdef CUresult cuIpcOpenMemHandle(CUdeviceptr* pdptr, CUipcMemHandle handle, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
418 return _driver._cuIpcOpenMemHandle_v2(pdptr, handle, Flags)
421cdef CUresult cuIpcCloseMemHandle(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
422 return _driver._cuIpcCloseMemHandle(dptr)
425cdef CUresult cuMemHostRegister(void* p, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
426 return _driver._cuMemHostRegister_v2(p, bytesize, Flags) 26q{x
429cdef CUresult cuMemHostUnregister(void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
430 return _driver._cuMemHostUnregister(p) 26q{x
433cdef CUresult cuMemcpy(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
434 return _driver._cuMemcpy(dst, src, ByteCount)
437cdef CUresult cuMemcpyPeer(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
438 return _driver._cuMemcpyPeer(dstDevice, dstContext, srcDevice, srcContext, ByteCount)
441cdef CUresult cuMemcpyHtoD(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
442 return _driver._cuMemcpyHtoD_v2(dstDevice, srcHost, ByteCount) 2CybbWMXMYM
445cdef CUresult cuMemcpyDtoH(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
446 return _driver._cuMemcpyDtoH_v2(dstHost, srcDevice, ByteCount) 29 ! # - M P Cybb
449cdef CUresult cuMemcpyDtoD(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
450 return _driver._cuMemcpyDtoD_v2(dstDevice, srcDevice, ByteCount)
453cdef CUresult cuMemcpyDtoA(CUarray dstArray, size_t dstOffset, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
454 return _driver._cuMemcpyDtoA_v2(dstArray, dstOffset, srcDevice, ByteCount)
457cdef CUresult cuMemcpyAtoD(CUdeviceptr dstDevice, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
458 return _driver._cuMemcpyAtoD_v2(dstDevice, srcArray, srcOffset, ByteCount)
461cdef CUresult cuMemcpyHtoA(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
462 return _driver._cuMemcpyHtoA_v2(dstArray, dstOffset, srcHost, ByteCount)
465cdef CUresult cuMemcpyAtoH(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
466 return _driver._cuMemcpyAtoH_v2(dstHost, srcArray, srcOffset, ByteCount)
469cdef CUresult cuMemcpyAtoA(CUarray dstArray, size_t dstOffset, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
470 return _driver._cuMemcpyAtoA_v2(dstArray, dstOffset, srcArray, srcOffset, ByteCount)
473cdef CUresult cuMemcpy2D(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
474 return _driver._cuMemcpy2D_v2(pCopy)
477cdef CUresult cuMemcpy2DUnaligned(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
478 return _driver._cuMemcpy2DUnaligned_v2(pCopy)
481cdef CUresult cuMemcpy3D(const CUDA_MEMCPY3D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
482 return _driver._cuMemcpy3D_v2(pCopy)
485cdef CUresult cuMemcpy3DPeer(const CUDA_MEMCPY3D_PEER* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
486 return _driver._cuMemcpy3DPeer(pCopy)
489cdef CUresult cuMemcpyAsync(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
490 return _driver._cuMemcpyAsync(dst, src, ByteCount, hStream) 2y $ z x D abE F R S T ) ` ng.iebfb. VbWbXbgbhbibjbkblbMbX Y Nb|ixe}d~dYbmbZbO
493cdef CUresult cuMemcpyPeerAsync(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
494 return _driver._cuMemcpyPeerAsync(dstDevice, dstContext, srcDevice, srcContext, ByteCount, hStream)
497cdef CUresult cuMemcpyHtoDAsync(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
498 return _driver._cuMemcpyHtoDAsync_v2(dstDevice, srcHost, ByteCount, hStream) 2AsBs1lCsDsEq
501cdef CUresult cuMemcpyDtoHAsync(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
502 return _driver._cuMemcpyDtoHAsync_v2(dstHost, srcDevice, ByteCount, hStream) 2AsBs1lDqCsDs{d|deg
505cdef CUresult cuMemcpyDtoDAsync(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
506 return _driver._cuMemcpyDtoDAsync_v2(dstDevice, srcDevice, ByteCount, hStream)
509cdef CUresult cuMemcpyHtoAAsync(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
510 return _driver._cuMemcpyHtoAAsync_v2(dstArray, dstOffset, srcHost, ByteCount, hStream)
513cdef CUresult cuMemcpyAtoHAsync(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
514 return _driver._cuMemcpyAtoHAsync_v2(dstHost, srcArray, srcOffset, ByteCount, hStream)
517cdef CUresult cuMemcpy2DAsync(const CUDA_MEMCPY2D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
518 return _driver._cuMemcpy2DAsync_v2(pCopy, hStream)
521cdef CUresult cuMemcpy3DAsync(const CUDA_MEMCPY3D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
522 return _driver._cuMemcpy3DAsync_v2(pCopy, hStream) 2Z ijjjhg
525cdef CUresult cuMemcpy3DPeerAsync(const CUDA_MEMCPY3D_PEER* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
526 return _driver._cuMemcpy3DPeerAsync(pCopy, hStream)
529cdef CUresult cuMemsetD8(CUdeviceptr dstDevice, unsigned char uc, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
530 return _driver._cuMemsetD8_v2(dstDevice, uc, N)
533cdef CUresult cuMemsetD16(CUdeviceptr dstDevice, unsigned short us, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
534 return _driver._cuMemsetD16_v2(dstDevice, us, N)
537cdef CUresult cuMemsetD32(CUdeviceptr dstDevice, unsigned int ui, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
538 return _driver._cuMemsetD32_v2(dstDevice, ui, N)
541cdef CUresult cuMemsetD2D8(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
542 return _driver._cuMemsetD2D8_v2(dstDevice, dstPitch, uc, Width, Height)
545cdef CUresult cuMemsetD2D16(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
546 return _driver._cuMemsetD2D16_v2(dstDevice, dstPitch, us, Width, Height)
549cdef CUresult cuMemsetD2D32(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
550 return _driver._cuMemsetD2D32_v2(dstDevice, dstPitch, ui, Width, Height)
553cdef CUresult cuMemsetD8Async(CUdeviceptr dstDevice, unsigned char uc, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
554 return _driver._cuMemsetD8Async(dstDevice, uc, N, hStream) 2M P y $ z x 6p9p#p$p%p-p.p?p]p_p`p{pdqeqjqmqoqpqqqxqyq
557cdef CUresult cuMemsetD16Async(CUdeviceptr dstDevice, unsigned short us, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
558 return _driver._cuMemsetD16Async(dstDevice, us, N, hStream) 27p'p(p)p/p:p@p|p}p~pfqgqkqrqsqtqzqAq
561cdef CUresult cuMemsetD32Async(CUdeviceptr dstDevice, unsigned int ui, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
562 return _driver._cuMemsetD32Async(dstDevice, ui, N, hStream) 28p!p*p+p,p;p=p[p^paqbqcqhqiqlqnquqvqwqBqCq
565cdef CUresult cuMemsetD2D8Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
566 return _driver._cuMemsetD2D8Async(dstDevice, dstPitch, uc, Width, Height, hStream)
569cdef CUresult cuMemsetD2D16Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
570 return _driver._cuMemsetD2D16Async(dstDevice, dstPitch, us, Width, Height, hStream)
573cdef CUresult cuMemsetD2D32Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
574 return _driver._cuMemsetD2D32Async(dstDevice, dstPitch, ui, Width, Height, hStream)
577cdef CUresult cuArrayCreate(CUarray* pHandle, const CUDA_ARRAY_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
578 return _driver._cuArrayCreate_v2(pHandle, pAllocateArray) 2t1
581cdef CUresult cuArrayGetDescriptor(CUDA_ARRAY_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
582 return _driver._cuArrayGetDescriptor_v2(pArrayDescriptor, hArray)
585cdef CUresult cuArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUarray array) except ?CUDA_ERROR_NOT_FOUND nogil:
586 return _driver._cuArrayGetSparseProperties(sparseProperties, array)
589cdef CUresult cuMipmappedArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUmipmappedArray mipmap) except ?CUDA_ERROR_NOT_FOUND nogil:
590 return _driver._cuMipmappedArrayGetSparseProperties(sparseProperties, mipmap)
593cdef CUresult cuArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUarray array, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
594 return _driver._cuArrayGetMemoryRequirements(memoryRequirements, array, device)
597cdef CUresult cuMipmappedArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUmipmappedArray mipmap, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
598 return _driver._cuMipmappedArrayGetMemoryRequirements(memoryRequirements, mipmap, device)
601cdef CUresult cuArrayGetPlane(CUarray* pPlaneArray, CUarray hArray, unsigned int planeIdx) except ?CUDA_ERROR_NOT_FOUND nogil:
602 return _driver._cuArrayGetPlane(pPlaneArray, hArray, planeIdx)
605cdef CUresult cuArrayDestroy(CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
606 return _driver._cuArrayDestroy(hArray) 2t1)rBMCMDMEMFMGMZ HMod0pijjj,r-rMM.r:rNMOMPMQMRMSMLh
609cdef CUresult cuArray3DCreate(CUarray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
610 return _driver._cuArray3DCreate_v2(pHandle, pAllocateArray) 2)rBMCMDMEMFMGMZ HMod0pijjj,r-rMM.r:rNMOMPMQMRMSMLh
613cdef CUresult cuArray3DGetDescriptor(CUDA_ARRAY3D_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
614 return _driver._cuArray3DGetDescriptor_v2(pArrayDescriptor, hArray) 2*r+rhg
617cdef CUresult cuMipmappedArrayCreate(CUmipmappedArray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc, unsigned int numMipmapLevels) except ?CUDA_ERROR_NOT_FOUND nogil:
618 return _driver._cuMipmappedArrayCreate(pHandle, pMipmappedArrayDesc, numMipmapLevels) 2IM*rJM+rhgKMLM/rLh
621cdef CUresult cuMipmappedArrayGetLevel(CUarray* pLevelArray, CUmipmappedArray hMipmappedArray, unsigned int level) except ?CUDA_ERROR_NOT_FOUND nogil:
622 return _driver._cuMipmappedArrayGetLevel(pLevelArray, hMipmappedArray, level) 2*r+rhg
625cdef CUresult cuMipmappedArrayDestroy(CUmipmappedArray hMipmappedArray) except ?CUDA_ERROR_NOT_FOUND nogil:
626 return _driver._cuMipmappedArrayDestroy(hMipmappedArray) 2IM*rJM+rhgKMLM/rLh
629cdef CUresult cuMemGetHandleForAddressRange(void* handle, CUdeviceptr dptr, size_t size, CUmemRangeHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
630 return _driver._cuMemGetHandleForAddressRange(handle, dptr, size, handleType, flags)
633cdef CUresult cuMemBatchDecompressAsync(CUmemDecompressParams* paramsArray, size_t count, unsigned int flags, size_t* errorIndex, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
634 return _driver._cuMemBatchDecompressAsync(paramsArray, count, flags, errorIndex, stream)
637cdef CUresult cuMemAddressReserve(CUdeviceptr* ptr, size_t size, size_t alignment, CUdeviceptr addr, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
638 return _driver._cuMemAddressReserve(ptr, size, alignment, addr, flags) 2md0bcbnd
641cdef CUresult cuMemAddressFree(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
642 return _driver._cuMemAddressFree(ptr, size) 2md0bcbnd
645cdef CUresult cuMemCreate(CUmemGenericAllocationHandle* handle, size_t size, const CUmemAllocationProp* prop, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
646 return _driver._cuMemCreate(handle, size, prop, flags) 2md0bcbnd
649cdef CUresult cuMemRelease(CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
650 return _driver._cuMemRelease(handle) 2md0bcbnd
653cdef CUresult cuMemMap(CUdeviceptr ptr, size_t size, size_t offset, CUmemGenericAllocationHandle handle, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
654 return _driver._cuMemMap(ptr, size, offset, handle, flags) 2md0bcbnd
657cdef CUresult cuMemMapArrayAsync(CUarrayMapInfo* mapInfoList, unsigned int count, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
658 return _driver._cuMemMapArrayAsync(mapInfoList, count, hStream)
661cdef CUresult cuMemUnmap(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
662 return _driver._cuMemUnmap(ptr, size) 2md0bcbnd
665cdef CUresult cuMemSetAccess(CUdeviceptr ptr, size_t size, const CUmemAccessDesc* desc, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
666 return _driver._cuMemSetAccess(ptr, size, desc, count) 2md0bcbnd
669cdef CUresult cuMemGetAccess(unsigned long long* flags, const CUmemLocation* location, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
670 return _driver._cuMemGetAccess(flags, location, ptr)
673cdef CUresult cuMemExportToShareableHandle(void* shareableHandle, CUmemGenericAllocationHandle handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
674 return _driver._cuMemExportToShareableHandle(shareableHandle, handle, handleType, flags)
677cdef CUresult cuMemImportFromShareableHandle(CUmemGenericAllocationHandle* handle, void* osHandle, CUmemAllocationHandleType shHandleType) except ?CUDA_ERROR_NOT_FOUND nogil:
678 return _driver._cuMemImportFromShareableHandle(handle, osHandle, shHandleType)
681cdef CUresult cuMemGetAllocationGranularity(size_t* granularity, const CUmemAllocationProp* prop, CUmemAllocationGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil:
682 return _driver._cuMemGetAllocationGranularity(granularity, prop, option) 2md0bcbnd
685cdef CUresult cuMemGetAllocationPropertiesFromHandle(CUmemAllocationProp* prop, CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
686 return _driver._cuMemGetAllocationPropertiesFromHandle(prop, handle)
689cdef CUresult cuMemRetainAllocationHandle(CUmemGenericAllocationHandle* handle, void* addr) except ?CUDA_ERROR_NOT_FOUND nogil:
690 return _driver._cuMemRetainAllocationHandle(handle, addr) 2md0bcbnd
693cdef CUresult cuMemFreeAsync(CUdeviceptr dptr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
694 return _driver._cuMemFreeAsync(dptr, hStream) 2M ?b@b[bsdtdudy $ z x D abE F R S T SbTbUb% ' ( igaeZMiFvdkFmFjgkg1p2p3p4p5pteuedblgDyEyFyGyHyIyJyKyLyMymgNyve$hebfb. VbWbXb%h'hgbhbibjbkblb_g`gMbX Y [ipg]i^iYb3cqlmb_iDdrlEd4cFdec5c6cGdfcHdgcJe7cId2j{gKeslZbhcLeO zFQFTFLvMvNvOvKrLrPvQvRvSvTv-FUv.FVvWv/FXvYvZvfGvG#vvw[HPwQwRwSwOrPrTwUwVwWwXwsIYwtIZw0wuI1w2w3wOI4I(wzxfdgdAKSK!K[KjLBLTL#LZ odtlulvlwlxlylzlAlBlClDlEl|g}gFq)fXr*f+fYr,f-f.f/fZr0r:f1r2r;f3r=f?f4r@f[f5r]f6r^f_f`f{f7r|f8r9r}f!r#r~fagbgcgSpTpwd
697cdef CUresult cuMemAllocAsync(CUdeviceptr* dptr, size_t bytesize, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
698 return _driver._cuMemAllocAsync(dptr, bytesize, hStream) 2sdtdudy z x D E F R S T SbTbUb% ' (
701cdef CUresult cuMemPoolTrimTo(CUmemoryPool pool, size_t minBytesToKeep) except ?CUDA_ERROR_NOT_FOUND nogil:
702 return _driver._cuMemPoolTrimTo(pool, minBytesToKeep)
705cdef CUresult cuMemPoolSetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
706 return _driver._cuMemPoolSetAttribute(pool, attr, value) 2Oynb
709cdef CUresult cuMemPoolGetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
710 return _driver._cuMemPoolGetAttribute(pool, attr, value) 2M P ?b@b[by $ z x D abE F Oy_g`gMbX Y [ipg]i^iBA|C_i+hyeEd4c,hze-hAe.hqg/hBeFdec:hCe;h5crgsgtgug6cvg=hDeGdfc?hEe@hFe[hGe1jHeHdgc]hIewgxg^hJe7cId{gO 3j8j9jTe* UeKd8c9cLdaiMdNdOdVenb(j2b!cDgbiPdQd)jfiliZgrkgf+ hf8d=c?c9dHi!d#d$dif9bxk!b@cIiJi%d'dykDkPi?g!k(k-k=k^k}kdlilZ odtlulvlwlxlylzlAlBlClDlEl|g}g)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}f~fagbgcgSpTp
713cdef CUresult cuMemPoolSetAccess(CUmemoryPool pool, const CUmemAccessDesc* map, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
714 return _driver._cuMemPoolSetAccess(pool, map, count) 27z8z9z!z#z$z%z'zte(zue)z*z+zdblg,z-z.z/z:z;z=z?z@z[z]z^z_z`z{z|z}z~zaAbAcAdAeAmgfAgAhAve$hebfb. VbWbXb%h'hgbhbibjbkblbYb(t3c(h)h*hmbDd+hyeEd4c,hze-hAe.hqg/hBeFdec:hCe;h5crgsgtgug6cvg=hDeGdfc?hEe@hFe[hGe1jHeHdgc]hIewgxg^hJe7cId2jZbhcLe2m`h{hO QnRnSnTnfdgd
717cdef CUresult cuMemPoolGetAccess(CUmemAccess_flags* flags, CUmemoryPool memPool, CUmemLocation* location) except ?CUDA_ERROR_NOT_FOUND nogil:
718 return _driver._cuMemPoolGetAccess(flags, memPool, location) 2|C
721cdef CUresult cuMemPoolCreate(CUmemoryPool* pool, const CUmemPoolProps* poolProps) except ?CUDA_ERROR_NOT_FOUND nogil:
722 return _driver._cuMemPoolCreate(pool, poolProps) 2[L5xIp]LJp6x^L7x_L8xte`Lue9x{L!x|LOjmryr}L#x~LaMbMcMdMeMfMgMhMiMjMkM$x%x'x(x)x*x+x,x-xQj.x/xlM:xmM;xnM=xoMRjpM?x. VbqM@xrM[xsM]xgbhbibjbkblbOyYb(t3c(h)h*hmbDd+hyeEd4c,hze-hAe.hqg/hBeFdec:hCe;h5crgsgtgug6cvg=hDeGdfc?hEe@hFe[hGe1jHeHdgc]hIewgxg^hJe7cId2jZbhcLe2m`h{hQnRnSnTnfdgd
725cdef CUresult cuMemPoolDestroy(CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
726 return _driver._cuMemPoolDestroy(pool) 27z8z9z!z#z$z%z'zte(zue)z*z+zdblg,z-z.z/z:z;z=z?z@z[z]z^z_z`z{z|z}z~zaAbAcAdAeAmgfAgAhAve$hebfb. VbWbXb%h'hgbhbibjbkblbOyYb(t3c(h)h*hmbDd+hyeEd4c,hze-hAe.hqg/hBeFdec:hCe;h5crgsgtgug6cvg=hDeGdfc?hEe@hFe[hGe1jHeHdgc]hIewgxg^hJe7cId2jZbhcLe2m`h{hO QnRnSnTnfdgd
729cdef CUresult cuMemAllocFromPoolAsync(CUdeviceptr* dptr, size_t bytesize, CUmemoryPool pool, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
730 return _driver._cuMemAllocFromPoolAsync(dptr, bytesize, pool, hStream) 2M P ?b@b[by $ z x D abE F igaeZMLjvdMjNjjgkg1p2p3p4p5pIpJp1q?u@u[uteue) ` PjlgDyEyFyGyHyIyJyKyLyMymgNy2q]u^uve3q$hng.iebfb. VbWbXb%h'h4q_ugbhbibjbkblb_g`gMbX Y [ipg]i^iYb3cqlmb_iDdrlEd4cFdec5c6cGdfcHdgcJe7cId2j{gKeslZbhcLeO 3j8j9jTe* UeKd8c9cLdaiMdNdOdVenb(j2b!cDgbiPdQd)jfiliZgrkgf+ hf8d=c?c9dHi!d#d$dif9bxk!b@cIiJi%d'dykDkPi?gfdgd!k(k-k=k^k}kdlilZ odtlulvlwlxlylzlAlBlClDlEl|g}gFq)fXr*f+fYr,f-f.f/fZr0r:f1r2r;f3r=f?f4r@f[f5r]f6r^f_f`f{f7r|f8r9r}f!r#r~fagbgcgSpTpwd
733cdef CUresult cuMemPoolExportToShareableHandle(void* handle_out, CUmemoryPool pool, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
734 return _driver._cuMemPoolExportToShareableHandle(handle_out, pool, handleType, flags) 2[L5xIp]LJp6x^L7x_L8xte`Lue9x{L!x|LOjmryr}L#x~LaMbMcMdMeMfMgMhMiMjMkM$x%x'x(x)x*x+x,x-xQj.x/xlM:xmM;xnM=xoMRjpM?x. VbqM@xrM[xsM]xgbhbibjbkblbye4czeAeqgBeecCeDefcEeFeGeHegcIehc`h{hQnRnSnTnfdgd
737cdef CUresult cuMemPoolImportFromShareableHandle(CUmemoryPool* pool_out, void* handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
738 return _driver._cuMemPoolImportFromShareableHandle(pool_out, handle, handleType, flags)
741cdef CUresult cuMemPoolExportPointer(CUmemPoolPtrExportData* shareData_out, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
742 return _driver._cuMemPoolExportPointer(shareData_out, ptr) 2IpJp1q?u@u[uteue) ` PjlgDyEyFyGyHyIyJyKyLyMymgNy2q]u^uve3q$hng.iebfb. VbWbXb%h'h4q_ugbhbibjbkblbhcfdgd
745cdef CUresult cuMemPoolImportPointer(CUdeviceptr* ptr_out, CUmemoryPool pool, CUmemPoolPtrExportData* shareData) except ?CUDA_ERROR_NOT_FOUND nogil:
746 return _driver._cuMemPoolImportPointer(ptr_out, pool, shareData)
749cdef CUresult cuMulticastCreate(CUmemGenericAllocationHandle* mcHandle, const CUmulticastObjectProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
750 return _driver._cuMulticastCreate(mcHandle, prop)
753cdef CUresult cuMulticastAddDevice(CUmemGenericAllocationHandle mcHandle, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
754 return _driver._cuMulticastAddDevice(mcHandle, dev)
757cdef 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:
758 return _driver._cuMulticastBindMem(mcHandle, mcOffset, memHandle, memOffset, size, flags)
761cdef CUresult cuMulticastBindAddr(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
762 return _driver._cuMulticastBindAddr(mcHandle, mcOffset, memptr, size, flags)
765cdef CUresult cuMulticastUnbind(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
766 return _driver._cuMulticastUnbind(mcHandle, dev, mcOffset, size)
769cdef CUresult cuMulticastGetGranularity(size_t* granularity, const CUmulticastObjectProp* prop, CUmulticastGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil:
770 return _driver._cuMulticastGetGranularity(granularity, prop, option)
773cdef CUresult cuPointerGetAttribute(void* data, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
774 return _driver._cuPointerGetAttribute(data, attribute, ptr) 29 ! # - degejemepeseFsNePeSe2bRdXeTd1eXd0d+e%ctb@e6 6b7buc*c+c,c-c5d6d~e;ccfff!b(dkfmfqf,d/dHf^cAbQf7 %b'bJc|c}c~cad@dWfYfed1f3f5f7f9f#f%f(fFqwd
777cdef CUresult cuMemPrefetchAsync(CUdeviceptr devPtr, size_t count, CUmemLocation location, unsigned int flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
778 return _driver._cuMemPrefetchAsync_v2(devPtr, count, location, flags, hStream) 2WlXlvdYlZl
781cdef CUresult cuMemAdvise(CUdeviceptr devPtr, size_t count, CUmem_advise advice, CUmemLocation location) except ?CUDA_ERROR_NOT_FOUND nogil:
782 return _driver._cuMemAdvise_v2(devPtr, count, advice, location) 2'sSmMqOqu1Es0M1MRp
785cdef CUresult cuMemRangeGetAttribute(void* data, size_t dataSize, CUmem_range_attribute attribute, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
786 return _driver._cuMemRangeGetAttribute(data, dataSize, attribute, devPtr, count) 2ae'sSmMqOqvdYlZlEs0M1MjgkgRp
789cdef 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:
790 return _driver._cuMemRangeGetAttributes(data, dataSizes, attributes, numAttributes, devPtr, count) 2Rp
793cdef CUresult cuPointerSetAttribute(const void* value, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
794 return _driver._cuPointerSetAttribute(value, attribute, ptr) 2Fs
797cdef CUresult cuPointerGetAttributes(unsigned int numAttributes, CUpointer_attribute* attributes, void** data, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
798 return _driver._cuPointerGetAttributes(numAttributes, attributes, data, ptr) 2U 4 c d e f g h i j k l m n o p q r H s t u v w I J K L Q N A B C b {bG 1 2 igae'sSmMqOqu1WlXlvdYlZl%r'rEs0M1Mjgkg`iFs]4MbX Y ihjhkh0c1clhmhnhoh2cphqhrhshfgthuhvhwhxhyhzhAhBhChDhEhFhGhHhSrTr[ipg^45q^x_x`x6q{xpl3c{gKeO Fq_4`4{4|4}4~4a5b5c5d5
801cdef CUresult cuStreamCreate(CUstream* phStream, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
802 return _driver._cuStreamCreate(phStream, Flags) 2lj2MMhbb1lDqEqv1{d|d:i;i=ieg?i@i
805cdef CUresult cuStreamCreateWithPriority(CUstream* phStream, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil:
806 return _driver._cuStreamCreateWithPriority(phStream, flags, priority) 2bjObPbggU (b{ cjV Ucdj8 4 ay, Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L pdhdidjd]d5 ]bqdrdDbEbFb*bGb9 ! # - +b,b-bVckd^b_bQbRbM P 0 | } `bQ N A B C b ?b@b[bsdtdudy $ z x D abE F R S T SbTbUb% ' ( G 1 2 Lb:b;bld=bW igaeWlXlvdYlZl%r'rjgkg1p2p3p4p5p`i) ` KpLpMpdbNp-iOpPp0lTMUMng.iebfb. VbWbXbgbhbibjbkblbbycydyeyfygyhyYc3 ZcIlJlKlLlMlNl~ OlPlQlRlSlgjJhWc~gUpahbhSjchdheh{ifhghhhFlNb|ixedchj}d~d;r=r6p?r7p@r[r8p9p]r^r_r!p`r#p$p%p'p(p)p*p+p,p{r-p.p/p:p|r;p=p}r~rasbs?pcs@pdses[p]pfsgshs^pis_p`p{p|p}p~paqbqcqjsdqeqfqgqkshqiqlsmsnsosjqpskqqsrslqmqsstsusnqvsoqpqqqrqsqtquqvqwqwsxqyqzqAqxsBqCqyszsYbmb_hZbTlUlO }i?t@t[t'qyiZgubpk|t0g+q1g2g3g,qziAiBiCi:c}t;cafqk-qDiEi~tcu5i?gBb9kgu@g_q[g]g^g`q6i7i8i9iddhuedZf%o{q!i#iXc[dmunuoupuquruuuxujykylymynyoy$rpyqyrysytyuyvywyxyVlyyWr(rzyKhAyZ od0pijjjhgwd
809cdef CUresult cuStreamGetPriority(CUstream hStream, int* priority) except ?CUDA_ERROR_NOT_FOUND nogil:
810 return _driver._cuStreamGetPriority(hStream, priority)
813cdef CUresult cuStreamGetDevice(CUstream hStream, CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil:
814 return _driver._cuStreamGetDevice(hStream, device)
817cdef CUresult cuStreamGetFlags(CUstream hStream, unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
818 return _driver._cuStreamGetFlags(hStream, flags)
821cdef CUresult cuStreamGetId(CUstream hStream, unsigned long long* streamId) except ?CUDA_ERROR_NOT_FOUND nogil:
822 return _driver._cuStreamGetId(hStream, streamId)
825cdef CUresult cuStreamGetCtx(CUstream hStream, CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
826 return _driver._cuStreamGetCtx(hStream, pctx)
829cdef CUresult cuStreamGetCtx_v2(CUstream hStream, CUcontext* pCtx, CUgreenCtx* pGreenCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
830 return _driver._cuStreamGetCtx_v2(hStream, pCtx, pGreenCtx)
833cdef CUresult cuStreamWaitEvent(CUstream hStream, CUevent hEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
834 return _driver._cuStreamWaitEvent(hStream, hEvent, Flags) 2{ V 8 c d e f g h i j k l m n o p q r s t u v w W Khwd
837cdef CUresult cuStreamAddCallback(CUstream hStream, CUstreamCallback callback, void* userData, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
838 return _driver._cuStreamAddCallback(hStream, callback, userData, flags)
841cdef CUresult cuStreamBeginCapture(CUstream hStream, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil:
842 return _driver._cuStreamBeginCapture_v2(hStream, mode) 2bjObPbggU (b{ cjV Ucdj8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L ?b@b[bsdtdudy z x D E F R S T SbTbUb% ' ( G 1 Lb:b;bld=bW Z
845cdef CUresult cuStreamBeginCaptureToGraph(CUstream hStream, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil:
846 return _driver._cuStreamBeginCaptureToGraph(hStream, hGraph, dependencies, dependencyData, numDependencies, mode) 1cdefghijklmnopqrHstuvwIJKLGW
849cdef CUresult cuThreadExchangeStreamCaptureMode(CUstreamCaptureMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
850 return _driver._cuThreadExchangeStreamCaptureMode(mode)
853cdef CUresult cuStreamEndCapture(CUstream hStream, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
854 return _driver._cuStreamEndCapture(hStream, phGraph) 2bjObPbggU (b{ cjV Ucdj8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L ?b@b[bsdtdudy z x D E F R S T SbTbUb% ' ( G 1 Lb:b;bld=bW Z
857cdef CUresult cuStreamIsCapturing(CUstream hStream, CUstreamCaptureStatus* captureStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
858 return _driver._cuStreamIsCapturing(hStream, captureStatus) 2M P ?b@b[bsdtdudy $ z x D abE F R S T SbTbUb% ' ( igaeZMLjvdMjNjjgkg1p2p3p4p5pIpJp1q?u@u[uteue) ` PjlgDyEyFyGyHyIyJyKyLyMymgNy2q]u^uve3q$hng.iebfb. VbWbXb%h'h4q_ugbhbibjbkblb_g`gMbX Y [ipg]i^iYb3cqlmb_iDdrlEd4cFdec5c6cGdfcHdgcJe7cId2j{gKeslZbhcLeO 3j8j9jTe* UeKd8c9cLdaiMdNdOdVenb(j2b!cDgbiPdQd)jfiliZgrkgf+ hf8d=c?c9dHi!d#d$dif9bxk!b@cIiJi%d'dykDkPi?gfdgd!k(k-k=k^k}kdlilZ odtlulvlwlxlylzlAlBlClDlEl|g}gFq)fXr*f+fYr,f-f.f/fZr0r:f1r2r;f3r=f?f4r@f[f5r]f6r^f_f`f{f7r|f8r9r}f!r#r~fagbgcgSpTpwd
861cdef 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:
862 return _driver._cuStreamGetCaptureInfo_v3(hStream, captureStatus_out, id_out, graph_out, dependencies_out, edgeData_out, numDependencies_out) 2bjObPbggU (b{ cjV Ucdj8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L ?b@b[bsdtdudy z x D E F R S T SbTbUb% ' ( G 1 Lb:b;bld=bW Z
865cdef CUresult cuStreamUpdateCaptureDependencies(CUstream hStream, CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
866 return _driver._cuStreamUpdateCaptureDependencies_v2(hStream, dependencies, dependencyData, numDependencies, flags) 1UcdefghijklmnopqrHstuvwIJKLGW
869cdef CUresult cuStreamAttachMemAsync(CUstream hStream, CUdeviceptr dptr, size_t length, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
870 return _driver._cuStreamAttachMemAsync(hStream, dptr, length, flags)
873cdef CUresult cuStreamQuery(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
874 return _driver._cuStreamQuery(hStream)
877cdef CUresult cuStreamSynchronize(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
878 return _driver._cuStreamSynchronize(hStream) 2ObPbU V Uc4 , Cbc d e f g h i j k l m n o p q r H s t u v w I J K L pdhdidjd]d5 ]bqdrdDbEbFb*bGb9 ! # - +b,b-bVckd^b_bQbRbM P 0 | } `bQ N A B C b {by $ z x D abE F R S T SbTbUb% ' ( G 1 2 igaeWlXlvdYlZljgkgdbbbAsBs1lDqCsDsEqYc3 Zc~ MbX Y kjNb{d|d:i;i=ieg?i@idchjihjhkh0c1clhmhnhoh2cphqhrhshfgthuhvhwhxhyhzhAhBhChDhEhFhGhHhe5TlUlO (rKhZ ijjjhgFqwd
881cdef CUresult cuStreamDestroy(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
882 return _driver._cuStreamDestroy_v2(hStream) 2bjObPbggU (b{ cjV Ucdj8 4 ay, Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L pdhdidjd]d5 ]bqdrdDbEbFb*bGb9 ! # - +b,b-bVcGqkd^b_bQbRbM P 0 | } `bQ N A B C b ?b@b[bsdtdudy $ z x D abE F R S T SbTbUb% ' ( G 1 2 Lb:b;bld=bW igaeWlXlvdYlZl%r'rjgkg1p2p3p4p5p`idb-i0lTMUMPjmgveebfb. WbXbgbhbibjbkblbbycydyeyfygylj2MMhbb1lDqEqhyYc3 ZcIlJlKlLlMlNl~ OlPlQlRlSlgjJhWc~gahbhSjchdhehfhghhhByMbX Y VMkjNb|ixev1{d|d:i;i=ieg?i@idchj}d~d;r=r6p?r7p@r[r8p9p]r^r_r!p`r#p$p%p'p(p)p*p+p,p{r-p.p/p:p|r;p=p}r~rasbs?pcs@pdses[p]pfsgshs^pis_p`p{p|p}p~paqbqcqjsdqeqfqgqkshqiqlsmsnsosjqpskqqsrslqmqsstsusnqvsoqpqqqrqsqtquqvqwqwsxqyqzqAqxsBqCqyszsYbmbZbTlUlO }iNFRF7FJGuwvwwwxw/HywzwMrNrAwBwCwDwEw:HFw;HGwHw=HIwJwKwfI+IyxzxAxBxuKCxDxQrRrExFxGxHxIxvKJxwKKxLxxKMxNxOxXc[dOK6K;KfLxLPL7L=Ljykylymynyoy$rpyqyrysytyuyvywyxyVlyyWr(rzyKhAyZ od0pijjjhgwd
885cdef CUresult cuStreamCopyAttributes(CUstream dst, CUstream src) except ?CUDA_ERROR_NOT_FOUND nogil:
886 return _driver._cuStreamCopyAttributes(dst, src)
889cdef CUresult cuStreamGetAttribute(CUstream hStream, CUstreamAttrID attr, CUstreamAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
890 return _driver._cuStreamGetAttribute(hStream, attr, value_out)
893cdef CUresult cuStreamSetAttribute(CUstream hStream, CUstreamAttrID attr, const CUstreamAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
894 return _driver._cuStreamSetAttribute(hStream, attr, value)
897cdef CUresult cuEventCreate(CUevent* phEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
898 return _driver._cuEventCreate(phEvent, Flags) 2{ V 8 c d e f g h i j k l m n o p q r s t u v w ]bbeceeefeheiekeleneoeqereIh_dejQbRb`dfj0 W ) ` KpLpMpdbNp-iOpPp0lxMYc3 ZcyMWmzMIlJlKlLlMlNl~ OlPlQlRlSlgjJhWckjw1}iEA5j6jIA#j$jQeRe8c9cobpb~iFg+j,j]thiiiUdVd]jli5b-nPAmi^j_jni`t`j{j|j}jWdQAXdKg.n{t~jakoipi4e5e6e7eqi8e9e!e#eYdZdckdk1d2d'c(cikjk6b7b.c/c`e{enkVp+q1g2gUAtkukdfef=c?cvbwb!g#gAkBkZAFkGk)d*dJkPi$bMo2AQiKkLkRiduMkNkOkPk+d3A,d(g?qeuQkRkSiTitfufvfwfUixfyfzfAf-d.dTkUk:d;d_c`cZk0k%b'bbdcd;g=g6k7k_q[g]gXc[d8A$k%k#A*k+k(A/k:k,A@k[k:A`k{k@Aalbl^Aflgl{AklllVlKhwd
901cdef CUresult cuEventRecord(CUevent hEvent, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
902 return _driver._cuEventRecord(hEvent, hStream) 2{ V 8 c d e f g h i j k l m n o p q r s t u v w W ) ` KpLpMpdbNp-iOpPp0lYc3 ZcIlJlKlLlMlNl~ OlPlQlRlSlgjJhWckj}iXc[dVlKhwd
905cdef CUresult cuEventRecordWithFlags(CUevent hEvent, CUstream hStream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
906 return _driver._cuEventRecordWithFlags(hEvent, hStream, flags)
909cdef CUresult cuEventQuery(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
910 return _driver._cuEventQuery(hEvent) 2Ih_d`d~ gjJh
913cdef CUresult cuEventSynchronize(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
914 return _driver._cuEventSynchronize(hEvent) 23 ~ JhWckj
917cdef CUresult cuEventDestroy(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
918 return _driver._cuEventDestroy_v2(hEvent) 2{ V 8 c d e f g h i j k l m n o p q r s t u v w svtvuvvvwvxvyvzvAvBvCvDvEvGqIh_dej`dfjW db-i0lxMYc3 ZcyMWmzMIlJlKlLlMlNl~ OlPlQlRlSlgjJhWckjw1}iDFFvGvXFHvIvJvKvKrLr0v1v2v3v4v5vzG6v7v8v9v!v#v$v%vXG'v(v)v*v+v,v-v.vYG/vZG:v;v0G=v?v@v[v]v^v_v`v{v|v}v~vawbwcwdwewfwgwhwiwjwkwlwmwnwowpwqwrwswtwzwMrNr`HLwMwNwOwOrPr4w5w6w7w8w9w8I!w#w$w%w'w(w)w*w`I+w,w-w.w/w:w;w=w{I?w|I@w[w}I]w^w_w`w{w|w}w~waxbxcxdxexfxgxhxixjxkxlxmxnxoxpxqxrxsxtxuxvxwxxxDxQrRrXc[dEKPxQxWKRxSx'KTxUx`KVxWxnLXxYxFLZx0xXL1x2x(L3x4xVlKhwd
921cdef CUresult cuEventElapsedTime(float* pMilliseconds, CUevent hStart, CUevent hEnd) except ?CUDA_ERROR_NOT_FOUND nogil:
922 return _driver._cuEventElapsedTime_v2(pMilliseconds, hStart, hEnd) 2Yc3 ZcWc
925cdef CUresult cuImportExternalMemory(CUexternalMemory* extMem_out, const CUDA_EXTERNAL_MEMORY_HANDLE_DESC* memHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
926 return _driver._cuImportExternalMemory(extMem_out, memHandleDesc)
929cdef CUresult cuExternalMemoryGetMappedBuffer(CUdeviceptr* devPtr, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_BUFFER_DESC* bufferDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
930 return _driver._cuExternalMemoryGetMappedBuffer(devPtr, extMem, bufferDesc)
933cdef CUresult cuExternalMemoryGetMappedMipmappedArray(CUmipmappedArray* mipmap, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC* mipmapDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
934 return _driver._cuExternalMemoryGetMappedMipmappedArray(mipmap, extMem, mipmapDesc)
937cdef CUresult cuDestroyExternalMemory(CUexternalMemory extMem) except ?CUDA_ERROR_NOT_FOUND nogil:
938 return _driver._cuDestroyExternalMemory(extMem)
941cdef CUresult cuImportExternalSemaphore(CUexternalSemaphore* extSem_out, const CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC* semHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
942 return _driver._cuImportExternalSemaphore(extSem_out, semHandleDesc)
945cdef CUresult cuSignalExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
946 return _driver._cuSignalExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream)
949cdef CUresult cuWaitExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
950 return _driver._cuWaitExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream)
953cdef CUresult cuDestroyExternalSemaphore(CUexternalSemaphore extSem) except ?CUDA_ERROR_NOT_FOUND nogil:
954 return _driver._cuDestroyExternalSemaphore(extSem)
957cdef CUresult cuStreamWaitValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
958 return _driver._cuStreamWaitValue32_v2(stream, addr, value, flags)
961cdef CUresult cuStreamWaitValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
962 return _driver._cuStreamWaitValue64_v2(stream, addr, value, flags)
965cdef CUresult cuStreamWriteValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
966 return _driver._cuStreamWriteValue32_v2(stream, addr, value, flags)
969cdef CUresult cuStreamWriteValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
970 return _driver._cuStreamWriteValue64_v2(stream, addr, value, flags)
973cdef CUresult cuStreamBatchMemOp(CUstream stream, unsigned int count, CUstreamBatchMemOpParams* paramArray, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
974 return _driver._cuStreamBatchMemOp_v2(stream, count, paramArray, flags)
977cdef CUresult cuFuncGetAttribute(int* pi, CUfunction_attribute attrib, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
978 return _driver._cuFuncGetAttribute(pi, attrib, hfunc)
981cdef CUresult cuFuncSetAttribute(CUfunction hfunc, CUfunction_attribute attrib, int value) except ?CUDA_ERROR_NOT_FOUND nogil:
982 return _driver._cuFuncSetAttribute(hfunc, attrib, value)
985cdef CUresult cuFuncSetCacheConfig(CUfunction hfunc, CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
986 return _driver._cuFuncSetCacheConfig(hfunc, config)
989cdef CUresult cuFuncGetModule(CUmodule* hmod, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
990 return _driver._cuFuncGetModule(hmod, hfunc)
993cdef CUresult cuFuncGetName(const char** name, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
994 return _driver._cuFuncGetName(name, hfunc) 2f5
997cdef CUresult cuFuncGetParamInfo(CUfunction func, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil:
998 return _driver._cuFuncGetParamInfo(func, paramIndex, paramOffset, paramSize)
1001cdef CUresult cuFuncIsLoaded(CUfunctionLoadingState* state, CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
1002 return _driver._cuFuncIsLoaded(state, function)
1005cdef CUresult cuFuncLoad(CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
1006 return _driver._cuFuncLoad(function)
1009cdef 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:
1010 return _driver._cuLaunchKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams, extra) 2{d|d:i;i=ieg?i@i
1013cdef CUresult cuLaunchKernelEx(const CUlaunchConfig* config, CUfunction f, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil:
1014 return _driver._cuLaunchKernelEx(config, f, kernelParams, extra) 2U (b{ V Uc8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L y $ z x D abE F R S T G 1 Lb:b;bld=bW ) ` 3 ~ WcMbX Y Nbdchjihjhkh0c1clhmhnhoh2cphqhrhshfgthuhvhwhxhyhzhAhBhChDhEhFhGhHhO
1017cdef 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:
1018 return _driver._cuLaunchCooperativeKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams)
1021cdef CUresult cuLaunchCooperativeKernelMultiDevice(CUDA_LAUNCH_PARAMS* launchParamsList, unsigned int numDevices, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1022 return _driver._cuLaunchCooperativeKernelMultiDevice(launchParamsList, numDevices, flags)
1025cdef CUresult cuLaunchHostFunc(CUstream hStream, CUhostFn fn, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil:
1026 return _driver._cuLaunchHostFunc(hStream, fn, userData) 2ObPb
1029cdef CUresult cuFuncSetBlockShape(CUfunction hfunc, int x, int y, int z) except ?CUDA_ERROR_NOT_FOUND nogil:
1030 return _driver._cuFuncSetBlockShape(hfunc, x, y, z)
1033cdef CUresult cuFuncSetSharedSize(CUfunction hfunc, unsigned int bytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1034 return _driver._cuFuncSetSharedSize(hfunc, bytes)
1037cdef CUresult cuParamSetSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1038 return _driver._cuParamSetSize(hfunc, numbytes)
1041cdef CUresult cuParamSeti(CUfunction hfunc, int offset, unsigned int value) except ?CUDA_ERROR_NOT_FOUND nogil:
1042 return _driver._cuParamSeti(hfunc, offset, value)
1045cdef CUresult cuParamSetf(CUfunction hfunc, int offset, float value) except ?CUDA_ERROR_NOT_FOUND nogil:
1046 return _driver._cuParamSetf(hfunc, offset, value)
1049cdef CUresult cuParamSetv(CUfunction hfunc, int offset, void* ptr, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1050 return _driver._cuParamSetv(hfunc, offset, ptr, numbytes)
1053cdef CUresult cuLaunch(CUfunction f) except ?CUDA_ERROR_NOT_FOUND nogil:
1054 return _driver._cuLaunch(f)
1057cdef CUresult cuLaunchGrid(CUfunction f, int grid_width, int grid_height) except ?CUDA_ERROR_NOT_FOUND nogil:
1058 return _driver._cuLaunchGrid(f, grid_width, grid_height)
1061cdef CUresult cuLaunchGridAsync(CUfunction f, int grid_width, int grid_height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1062 return _driver._cuLaunchGridAsync(f, grid_width, grid_height, hStream)
1065cdef CUresult cuParamSetTexRef(CUfunction hfunc, int texunit, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1066 return _driver._cuParamSetTexRef(hfunc, texunit, hTexRef)
1069cdef CUresult cuFuncSetSharedMemConfig(CUfunction hfunc, CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
1070 return _driver._cuFuncSetSharedMemConfig(hfunc, config)
1073cdef CUresult cuGraphCreate(CUgraph* phGraph, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1074 return _driver._cuGraphCreate(phGraph, flags) 2gzhzizjzkzlzmznzoz9loj!lpzpj#l$lqzrzsztzuzmjvzwzxzyz5 zzAzBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z%l'l|bqjbecerj(l)l*l+lxddeOhPhQhRh,l-l.l/l}bsjeefetj:l;l=l?lydgeShThUhVh@l[l]luj^l4zvj_l`l{lwj|lxj}l~lambm~byjheiezjcmdmemfmzdjeWhXhYhZhgmhmimjmacAjkeleBjkmlmmmnmAdme0h1h2h3hompmqmrmbcQpneoeCjsmtmumvmBdpe4h5h6h7hwmxmymzmccDjqereEjAmBmCmDmCdse8h9h!h#hEmFmGmFjHmGjImJmKmHjLmIjMmNmGqOmJjPmKjQmRm4lx1y1z1A1~xB1PyKsolvr^d5lkdWpXpYpZpHbIbJbKb^b_b.bIh_dejQbRb`dfjM P dg0 | } /b`bajQ N A B C 3MHq2l3lb 6l{b7l2 4MljGs5MHsIsQyRyMhbbSy6MC1Unic7q4j5j6j7jFAVnWnXnMeNe|hGAUrZn1njc9q!j#j$j%jJA2n3nVrOePe}hKA5n6n1bQeRe'jygzgAgJdSe~hBgCgTe* UeKd8c9cLdaiMdNdOdnb2b!cbiPdQdobpb3b/ : ; = ciqbEg~iFgGgdi7n8n#cRdHg#q9n!n#nkc$q*j+j,j-jLA$n%n'nWeXeeiMA)n*n.j4b+ngihiiiji^t/j:j;jSdTdIg_t?j@j[jrbUdVdkiYeZe0e$c1eJg2e3e]j5b-nmi^j_jni`t`j{j|jWdXdKg{t~jakoipi4e5e6e7eqi8e9e!e#esbYdZd$e%e'e0dLg(e)e/nlc(qbkckdkek:n;n=n*e+eriRA?n@nMgNgOgPg[n]n^n_n`nsimcQgRg1d2dSgfk,e-e.e/e%c:egk;e=enc'c(c)c3docpctbqcrcsc{ntc)qhkikjkkkSA|n}n~n?e@etiTAboco6 6b7buc*c+c,c-c? .c/c4d[e]e5d^e_elkvcuivi`e{ewidoTgUgVg|e6dWgfoXgYggowcmknkVpokhoiojo}e~exikoloyiubpk0g1g2g3g,qziAiBi:c;caf-qDiEimonoxc.qsktkukvkVAoopoqobfcfFiWAsoto8bdfefwk4g5g6g7dffGi7g8ggf+ hf8d=c?c9dHi!d#d$d9b!b@cJi%d'dvbwb#b@ [ ] ^ Kixb9g!g#g$gLiuovo[c(d%g:qwoxoyoyc;qzkAkBkCkXAzoAoBojfkfMiYADoEoFozc=qEkFkGkHk0AGoHoIolfmfNi1AKoLoIkyb)d*dOinfofpf]cqf'grfsfJk$bMoQiKkLkRiduMkNkOk+d,d(geuQkRkSiTitfufvfwfUixfyfzfAfzb-d.dBfCfDf/d)gEfFfNoAc@qSkTkUkVkOoPoQoGfHfVi4ARoSo*g+g,g-gToUoVoWoXoWiBc.g/g:d;d:gWkIfJfKfLf^cMfXkNfOfCc_c`c{c=dDcEcAbFcGcHcYoIc[qYkZk0k1k5AZo0o1oPfQfXi6A3o4o7 %b'bJc|c}c~cad_ bdcd?dRfSf@dTfUf5oKc2k3k;g=g4k]qYiZi0iVfWf1i^q2i3i7oLc5k6k7k8k8o9o!oXfYf4i#o$o5iBb9k@g[g]g^g`q6i7i8iddedZf{q!i#i'o(oMc|q#k$k%k'k9A)o*o+o0f1f$i!A-o.o/oNcar)k*k+k,k$A:o;o=o2f3f%i%A@o[o]oOccr.k/k:k;k)A^o_o`o4f5f'i*A|o}o~oPcer?k@k[k]k-Aapbpcp6f7f(i.AepfpgpQcgr_k`k{k|k;Ahpipjp8f9f)i=AlpmpnpRcir~kalblcl[Aopppqp!f#f*i]AsptpupSckrelflglhl_Avpwpxp$f%f+i`AzpApBpTclrjlklllml|ACpDpEp'f(f,i}AGpHp
1077cdef CUresult cuGraphAddKernelNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1078 return _driver._cuGraphAddKernelNode_v2(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 25 DbEbFb*bGb/inl|bxd}byd~bzdacAdbcBdccCd^dHbIbJbKb.bM P dg0 | } /bQ N A B C b 2 icMejcOe1bJd* nbobpb3b/ : ; = qb#ckcWe4bSdrb$c5bWdsblc*emc/enc'c(c)c3docpctbqcrcsctc?e6 ? vc|ewc}eub:cxcbf8b7d+ 9bvbwb#b@ [ ] ^ xb[cycjfzclfyb]c$b+dzbAcGfBcLfCc_c`c{c=dDcEcAbFcGcHcIcPf7 _ KcVfLcXfBbddMc0fNc2fOc4fPc6fQc8fRc!fSc$fTc'f
1081cdef CUresult cuGraphKernelNodeGetParams(CUgraphNode hNode, CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1082 return _driver._cuGraphKernelNodeGetParams_v2(hNode, nodeParams) 27MHbIbJbKb.b/bb
1085cdef CUresult cuGraphKernelNodeSetParams(CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1086 return _driver._cuGraphKernelNodeSetParams_v2(hNode, nodeParams)
1089cdef CUresult cuGraphAddMemcpyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1090 return _driver._cuGraphAddMemcpyNode(phGraphNode, hGraph, dependencies, numDependencies, copyParams, ctx) 29 ! # - degejemepeseNePeSe2bRdXeTd1eXd0d+e%ctb@e6 6b7buc*c+c,c-c5d6d~e;ccfff!b(dkfmfqf,d/dHf^cAbQf7 %b'bJc|c}c~cad@dWfYfed1f3f5f7f9f#f%f(f
1093cdef CUresult cuGraphMemcpyNodeGetParams(CUgraphNode hNode, CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1094 return _driver._cuGraphMemcpyNodeGetParams(hNode, nodeParams) 2bb
1097cdef CUresult cuGraphMemcpyNodeSetParams(CUgraphNode hNode, const CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1098 return _driver._cuGraphMemcpyNodeSetParams(hNode, nodeParams)
1101cdef 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:
1102 return _driver._cuGraphAddMemsetNode(phGraphNode, hGraph, dependencies, numDependencies, memsetParams, ctx) 29 ! # - +b,b-bVcOhPhQhRhShThUhVhWhXhYhZh0h1h2h3h4h5h6h7h8h9h!h#hb {b|h}h~h!cHgeiIgJgKgLgri:eqcti? .c/c4d[e]e5d^e_eWgxiafFiGi@c%gMiNi'g(g)gViMfFcXi_ bdcd?dRfSf@dTfUf1i4iZf$i%i'i(i)i*i+i,i
1105cdef CUresult cuGraphMemsetNodeGetParams(CUgraphNode hNode, CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1106 return _driver._cuGraphMemsetNodeGetParams(hNode, nodeParams) 1b
1109cdef CUresult cuGraphMemsetNodeSetParams(CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1110 return _driver._cuGraphMemsetNodeSetParams(hNode, nodeParams)
1113cdef CUresult cuGraphAddHostNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1114 return _driver._cuGraphAddHostNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2pdqdrd(l)l:l;lcmdmkmlmsmtmAmBm^b_b`bVn2nygMd3bdi$n/jYe`jpiqi$e:nMgNgOgPg,e3d|nuc4dTghozioo4g!d#bLizoGonfMkTiUiBfOo*g+g,g-gIf=dZoJc?dYi8o6i)o:o^oaphpopvpCp
1117cdef CUresult cuGraphHostNodeGetParams(CUgraphNode hNode, CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1118 return _driver._cuGraphHostNodeGetParams(hNode, nodeParams)
1121cdef CUresult cuGraphHostNodeSetParams(CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1122 return _driver._cuGraphHostNodeSetParams(hNode, nodeParams)
1125cdef CUresult cuGraphAddChildGraphNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1126 return _driver._cuGraphAddChildGraphNode(phGraphNode, hGraph, dependencies, numDependencies, childGraph) 2U 5 |b}b~bacbccc.b/bicjc1b* obpb3b/ : ; = qbkc4brb5bsblcmcnctc6 ? vcwcubxc8b+ vbwb#b@ [ ] ^ xbyczcyb$bzbAcBcCcIc7 _ KcLcBbMcNcOcPcQcRcScTc
1129cdef CUresult cuGraphChildGraphNodeGetGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1130 return _driver._cuGraphChildGraphNodeGetGraph(hNode, phGraph) 25 |b}b~bacbccc.b/bicjc1b* obpb3b/ : ; = qbkc4brb5bsblcmcnctc6 ? vcwcubxc8b+ vbwb#b@ [ ] ^ xbyczcyb$bzbAcBcCcIc7 _ KcLcBbMcNcOcPcQcRcScTc
1133cdef CUresult cuGraphAddEmptyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1134 return _driver._cuGraphAddEmptyNode(phGraphNode, hGraph, dependencies, numDependencies) 2ojpjmj9 ! # - srtrurqjdesjgeujvjwjxjyjjeAjmeQppeDjseFjGjHjIjGqJjKjPyolQ N A B C 3MHq2l3l6l7lljGsHsIsQyRySy6M4jNe!jPeSeKd2bEgRd*jXegiTd[jrbUdVdkiYeZe0e$c1eJg2e3emiXd0dbk+eRg%ctbhk@e6 6b7buc*c+c,c-c5dvi6dmk~e0g;cskcfff8d!b9g(dzkkfEkmfIkyb)d*dOinfofpf]cqf'grfsfQi,d/dSkHf/g^cAbYkQf7 %b'bJc|c}c~cad@d3kWf5kYf@ged#k1f)k3f.k5f?k7f_k9f~k#fel%fjl(f
1137cdef CUresult cuGraphAddEventRecordNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1138 return _driver._cuGraphAddEventRecordNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2]bbeeehekeneqeIh_dejQbRb0 5j#jQe8cob~i+jhiUd^joipi4e5e6e7eYdck1d'cik6b.c`enk1gtkdf=cvb!gAkFk)dKkSiTitfufvfwf-dTk:d_cZk%bbd;g6k[g$k*k/k@k`kalflkl
1141cdef CUresult cuGraphEventRecordNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1142 return _driver._cuGraphEventRecordNodeGetEvent(hNode, event_out)
1145cdef CUresult cuGraphEventRecordNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1146 return _driver._cuGraphEventRecordNodeSetEvent(hNode, event)
1149cdef CUresult cuGraphAddEventWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1150 return _driver._cuGraphAddEventWaitNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2]bcefeieleoereQbRb`dfj6j$jRe9cpbFg,jiiVd_joiqi8e9e!e#eZddk2d(cjk7b/c{eVp2gukef?cwb#gBkGk*dLkSiUixfyfzfAf.dUk;d`c0k'bcd=g7k]g%k+k:k[k{kblglll
1153cdef CUresult cuGraphEventWaitNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1154 return _driver._cuGraphEventWaitNodeGetEvent(hNode, event_out)
1157cdef CUresult cuGraphEventWaitNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1158 return _driver._cuGraphEventWaitNodeSetEvent(hNode, event)
1161cdef 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:
1162 return _driver._cuGraphAddExternalSemaphoresSignalNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
1165cdef CUresult cuGraphExternalSemaphoresSignalNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1166 return _driver._cuGraphExternalSemaphoresSignalNodeGetParams(hNode, params_out)
1169cdef CUresult cuGraphExternalSemaphoresSignalNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1170 return _driver._cuGraphExternalSemaphoresSignalNodeSetParams(hNode, nodeParams)
1173cdef 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:
1174 return _driver._cuGraphAddExternalSemaphoresWaitNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
1177cdef CUresult cuGraphExternalSemaphoresWaitNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_WAIT_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1178 return _driver._cuGraphExternalSemaphoresWaitNodeGetParams(hNode, params_out)
1181cdef CUresult cuGraphExternalSemaphoresWaitNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1182 return _driver._cuGraphExternalSemaphoresWaitNodeSetParams(hNode, nodeParams)
1185cdef 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:
1186 return _driver._cuGraphAddBatchMemOpNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
1189cdef CUresult cuGraphBatchMemOpNodeGetParams(CUgraphNode hNode, CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1190 return _driver._cuGraphBatchMemOpNodeGetParams(hNode, nodeParams_out)
1193cdef CUresult cuGraphBatchMemOpNodeSetParams(CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1194 return _driver._cuGraphBatchMemOpNodeSetParams(hNode, nodeParams)
1197cdef CUresult cuGraphExecBatchMemOpNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1198 return _driver._cuGraphExecBatchMemOpNodeSetParams(hGraphExec, hNode, nodeParams)
1201cdef CUresult cuGraphAddMemAllocNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUDA_MEM_ALLOC_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1202 return _driver._cuGraphAddMemAllocNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2bBcBnrJs`udB{u9loj!lpj#l$lorhdidjd]d9 ! # - +b,b-bVcprqrrrsrtrur%l'lqjbecerjxddeOhPhQhRh.l/lsjeefetjydgeShThUhVh]luj^lvj_l`l{lwj|lxj}l~lambmyjheiezjzdjeWhXhYhZhimjmAjkeleBjAdme0h1h2h3hqmrmQpneoeCjBdpe4h5h6h7hymzmDjqereEjCdse8h9h!h#hGmFjHmGjImJmKmHjLmIjMmNmOmJjPmKjQmRmolvrkd_d`dMhUn4j7jNe|h1n!j%jPe}h1bQeRe'jygzgAgJdSe~hBgCgTeKdLd2b!cciEgGgRdHg#n*j-jXeei.jgijiTdIg[jrbUdVdkiYeZe0e$c1eJg2e3e]jminiXdKgsbYdZd$e%e'e0dLg(e)e/nbkek+erisiRgSg%c:e)ctbqc{nhkkk@eti6 6b7buc*c+c,c-c? .c/c4d[e]e5d^e_elkviwi6dWggomkok~exiyi0g3g;cafnoskvkcfFi8bdfefwk4g5g6g7dffGi7g8ggf8d9d!b@cKi9g$g(d%gyozkCkkfMiFoEkHkmfNiIkyb)d*dOinfofpf]cqf'grfsfJkQiRi,d(gzb-d.dBfCfDf/d)gEfFfNoSkVkHfViWi/g:g^cMf{cAbFcYoYk1kQfXi7 %b'bJc|c}c~cad_ bdcd?dRfSf@dTfUf5o3k4kWf1i7o5k8kYf4i5i@g^gedZf(o#k'k1f$i/o)k,k3f%i]o.k;k5f'i~o?k]k7f(igp_k|k9f)inp~kcl#f*iupelhl%f+iBpjlml(f,i
1205cdef CUresult cuGraphMemAllocNodeGetParams(CUgraphNode hNode, CUDA_MEM_ALLOC_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1206 return _driver._cuGraphMemAllocNodeGetParams(hNode, params_out) 28M9M!M#M$M%M'M(M)M*M+M,M-M.M/M:M;M=M?M@M[M]M^MTyUyVyWyXyYyZy0y1y2y3y
1209cdef CUresult cuGraphAddMemFreeNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
1210 return _driver._cuGraphAddMemFreeNode(phGraphNode, hGraph, dependencies, numDependencies, dptr) 2nrorhdidjd]d9 ! # - +b,b-bVcrjtjzjBjCjEjKsMh7j%j'jLdGg-jjikinisbYdZd$e%e'e0dLg(e)eekSg)ckkwiok3gvkwk9d$gCkHkOiRizb-d.dBfCfDf/d)gEfFfVk:g{c1k4k8k^g'k,k;k]k|kclhlml
1213cdef CUresult cuGraphMemFreeNodeGetParams(CUgraphNode hNode, CUdeviceptr* dptr_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1214 return _driver._cuGraphMemFreeNodeGetParams(hNode, dptr_out)
1217cdef CUresult cuDeviceGraphMemTrim(CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
1218 return _driver._cuDeviceGraphMemTrim(device) 1%'(
1221cdef CUresult cuDeviceGetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1222 return _driver._cuDeviceGetGraphMemAttribute(device, attr, value) 2% ' ( g5Mh
1225cdef CUresult cuDeviceSetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1226 return _driver._cuDeviceSetGraphMemAttribute(device, attr, value) 1%'(
1229cdef CUresult cuGraphClone(CUgraph* phGraphClone, CUgraph originalGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1230 return _driver._cuGraphClone(phGraphClone, originalGraph) 2QbP |
1233cdef CUresult cuGraphNodeFindInClone(CUgraphNode* phNode, CUgraphNode hOriginalNode, CUgraph hClonedGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1234 return _driver._cuGraphNodeFindInClone(phNode, hOriginalNode, hClonedGraph)
1237cdef CUresult cuGraphNodeGetType(CUgraphNode hNode, CUgraphNodeType* type) except ?CUDA_ERROR_NOT_FOUND nogil:
1238 return _driver._cuGraphNodeGetType(hNode, type) 27M8M9M!M#M$M%M'M(M)M*M+M,M-M.M/M:M;M=M?M@M[M]M^MTyUyVyWyXyYyZy_M0y1y2y3yh5i5j5k5l5m5n5o5p5q5r5s5t5u5v5w5x5y5z5HbIbJbKb.b/bajb
1241cdef CUresult cuGraphGetNodes(CUgraph hGraph, CUgraphNode* nodes, size_t* numNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1242 return _driver._cuGraphGetNodes(hGraph, nodes, numNodes) 2}xmj7M8M9MA5!M#M$MB5C5D5%M'M(M)M*M+ME5F5G5H5I5J5K5L5M5,M-MN5.M/M:M;MO5P5Q5R5=M?M@M[M]M^MS5T5U5V5W5X5Y5Z5PyWpXpYpZpHbIbJbKb.b/bajQ N A B C b {b
1245cdef CUresult cuGraphGetRootNodes(CUgraph hGraph, CUgraphNode* rootNodes, size_t* numRootNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1246 return _driver._cuGraphGetRootNodes(hGraph, rootNodes, numRootNodes)
1249cdef CUresult cuGraphGetEdges(CUgraph hGraph, CUgraphNode* from_, CUgraphNode* to, CUgraphEdgeData* edgeData, size_t* numEdges) except ?CUDA_ERROR_NOT_FOUND nogil:
1250 return _driver._cuGraphGetEdges_v2(hGraph, from_, to, edgeData, numEdges) 205152535455565mjQ N A B C b {bGs
1253cdef CUresult cuGraphNodeGetDependencies(CUgraphNode hNode, CUgraphNode* dependencies, CUgraphEdgeData* edgeData, size_t* numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1254 return _driver._cuGraphNodeGetDependencies_v2(hNode, dependencies, edgeData, numDependencies) 2nrormjsrtrur/iTyUy75VyWyXyYy8595!5#5Zy_M0y1y2y3y$5%5'5(5)5*5+5,5ol0 B 2l3lb GsIs
1257cdef CUresult cuGraphNodeGetDependentNodes(CUgraphNode hNode, CUgraphNode* dependentNodes, CUgraphEdgeData* edgeData, size_t* numDependentNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1258 return _driver._cuGraphNodeGetDependentNodes_v2(hNode, dependentNodes, edgeData, numDependentNodes) 2mjTyUyVyWyXyYyZy_M0y1y2y3y-5.5/5:5;5=5A C Hq2l3lb 6l7lIs
1261cdef CUresult cuGraphAddDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1262 return _driver._cuGraphAddDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 2mjA B C Hq2l3lb 6l{b7l
1265cdef CUresult cuGraphRemoveDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1266 return _driver._cuGraphRemoveDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 2C Hq2l3lb
1269cdef CUresult cuGraphDestroyNode(CUgraphNode hNode) except ?CUDA_ERROR_NOT_FOUND nogil:
1270 return _driver._cuGraphDestroyNode(hNode) 2GqN A B {b6M
1273cdef CUresult cuGraphInstantiate(CUgraphExec* phGraphExec, CUgraph hGraph, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1274 return _driver._cuGraphInstantiateWithFlags(phGraphExec, hGraph, flags) 2QbP | ljMhbbSy
1277cdef CUresult cuGraphInstantiateWithParams(CUgraphExec* phGraphExec, CUgraph hGraph, CUDA_GRAPH_INSTANTIATE_PARAMS* instantiateParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1278 return _driver._cuGraphInstantiateWithParams(phGraphExec, hGraph, instantiateParams) 2ObPbggU (bV 8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L pdhdidjd]d5 ]bqdrdDbEbFb*bGb9 ! # - +b,b-bVcD1E1F1prqrrr^dkd^b_bRbM 0 } `bQ N A B C b ?b@b[bsdtdudy z x D E F R S T SbTbUb% ' ( G 1 2 Lb:b;b=bZ
1281cdef CUresult cuGraphExecGetFlags(CUgraphExec hGraphExec, cuuint64_t* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1282 return _driver._cuGraphExecGetFlags(hGraphExec, flags)
1285cdef CUresult cuGraphExecKernelNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1286 return _driver._cuGraphExecKernelNodeSetParams_v2(hGraphExec, hNode, nodeParams)
1289cdef CUresult cuGraphExecMemcpyNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1290 return _driver._cuGraphExecMemcpyNodeSetParams(hGraphExec, hNode, copyParams, ctx)
1293cdef CUresult cuGraphExecMemsetNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1294 return _driver._cuGraphExecMemsetNodeSetParams(hGraphExec, hNode, memsetParams, ctx)
1297cdef CUresult cuGraphExecHostNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1298 return _driver._cuGraphExecHostNodeSetParams(hGraphExec, hNode, nodeParams)
1301cdef CUresult cuGraphExecChildGraphNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1302 return _driver._cuGraphExecChildGraphNodeSetParams(hGraphExec, hNode, childGraph)
1305cdef CUresult cuGraphExecEventRecordNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1306 return _driver._cuGraphExecEventRecordNodeSetEvent(hGraphExec, hNode, event)
1309cdef CUresult cuGraphExecEventWaitNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1310 return _driver._cuGraphExecEventWaitNodeSetEvent(hGraphExec, hNode, event)
1313cdef CUresult cuGraphExecExternalSemaphoresSignalNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1314 return _driver._cuGraphExecExternalSemaphoresSignalNodeSetParams(hGraphExec, hNode, nodeParams)
1317cdef CUresult cuGraphExecExternalSemaphoresWaitNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1318 return _driver._cuGraphExecExternalSemaphoresWaitNodeSetParams(hGraphExec, hNode, nodeParams)
1321cdef CUresult cuGraphNodeSetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1322 return _driver._cuGraphNodeSetEnabled(hGraphExec, hNode, isEnabled)
1325cdef CUresult cuGraphNodeGetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int* isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1326 return _driver._cuGraphNodeGetEnabled(hGraphExec, hNode, isEnabled)
1329cdef CUresult cuGraphUpload(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1330 return _driver._cuGraphUpload(hGraphExec, hStream) 2V , pdhdidjd5 ]bqdrdDbEbFbGb9 ! # +b,b-b^b_b`by z x D E F R S T SbTbUb% ' (
1333cdef CUresult cuGraphLaunch(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1334 return _driver._cuGraphLaunch(hGraphExec, hStream) 2ObPbU V 4 , c d e f g h i j k l m n o p q r H s t u v w I J K L pdhdidjd]d5 ]bqdrdDbEbFb*bGb9 ! # - +b,b-bVckd^b_bQbRbM P 0 | } `bQ N A B C b y z x D E F R S T SbTbUb% ' ( G 1 2 MhbbZ
1337cdef CUresult cuGraphExecDestroy(CUgraphExec hGraphExec) except ?CUDA_ERROR_NOT_FOUND nogil:
1338 return _driver._cuGraphExecDestroy(hGraphExec) 2ObPbggU (bV 8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L pdhdidjd]d5 ]bqdrdDbEbFb*bGb9 ! # - +b,b-bVcD1E1F1prqrrr^dkd^b_bRbM 0 } `bQ N A B C b ?b@b[bsdtdudy z x D E F R S T SbTbUb% ' ( G 1 2 Lb:b;b=bljbbSyZ
1341cdef CUresult cuGraphDestroy(CUgraph hGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1342 return _driver._cuGraphDestroy(hGraph) 2bjObPbggU (b{ cjV Ucdj8 4 , Cb)bc d e f g h i j k l m n o p q r H s t u v w I J K L ~CaDbDcDdDeDfDgDhDiDjDkDlDmDnDoDpDqDrDsDtDmjuDvDwDxD5 yDsvzDADBDCDDDEDFDGDHDIDJDKDLDMDNDODPDQDRDSDTDUDVDWDXDYDZD0D|b1Dtvuv2D3D4D5D6D7D8D9D!D#D$D%D'D(D}b)Dvvwv*D+D,D-D.D/D:D;D=D?D@D[D]D^D_D`D{D|D}D~DaEbEcEdEeEfEgE~bhEiExvyvjEkElEmEnEoEpEqErEsEtEuEvEwExEacyEzEzvAvAEBECEDEEEFEGEHEIEJEKELEMENEOEbcPEQEBvCvRESETEUEVEWEXEYEZE0E1E2E3E4E5Ecc6E7EDvEv8E9E!E#E$E%E'E(E)E*E+E,E-E.E/E:E;E=E?E@E[E]E^E_E`EGq{E|E}E~EaFbF4lx1y1z1A1~xB1PyKsolvr^d5lkdWpXpYpZpHbIbJbKb^b_b.bIh_dejQbRb`dfjM P dg0 | } /b`bajQ N A B C 3MHq2l3lb 6l{b7l?b@b[bsdtdudy z x D E F R S T SbTbUb% ' ( G 1 2 Lb:b;bld=bW ljGs5MHsIsQyRyMhbbC1yFicAFBFCFFvGvEFFFGFHFIFJFKFLFMFOFPFSFjcUFVFWFHvIvYFZF0F1F2F3F4F5F6F8F9F1b!FJvKv#F$F%F'F(F)F*F+F,FLv* MvNvOvKrLrPvQvRvSvTvUvVvWvXvYvZvob0vpb1v3b:F/ ;F: =F; ?F= @F[Fqb]F^F2v3v_F`F{F|F}F~FaGbGcGdGeGkcgGhGiG4v5vjGkGlGmGnGoGpGqGrGsGtGuG4bwGxGyG6v7vAGBGCGDGEGFGGGHGIGKGLGMGrbNG8v9vOGPGQGRGSGTGUGVGWG!v5b$v%v'v(v)v*v+v,v-v.v/v:v;v=v?v@v[v]v^v_v`v{v|v}v~vawbwsb1Gcwdw2G3G4G5G6G7G8G9Glc!G#G$Gewfw%G'G(G)G*G+G,G-G.G/G:G;G=G?G@G[G]G^G_G`Gmc{G|G}Ggwhw~GaHbHcHdHeHfHgHhHiHjHnckHiwjwlHmHnHoHpHqHrHsHtHtcuHvHwHkwlwxHyHzHAHBHCHDHEHFHGHHH6 IHmwnwJHKHLHMHNH? OHowpwPHQHRHSHTHUHVHvcWHXHYHqwrwZH0H1H2H3H4H5H6H7H8H9H!Hwc#H$Hswtw%H'H(H)H*H+H,H-H.HuwubwwxwywMrNrAwBwCwDwEwFwGwHwIwJwKw?H@Hxc]H^H_HLwMw{H|H}H~HaIbIcIdIeIgIhI8biINwOwjIkIlImInIoIpIqIrIPw+ QwRwSwOrPrTwUwVwWwXwYwZw0w1w2w3wvb4wwb5w#bvI@ wI[ xI] yI^ zIAIxbBICI6w7wDIEIFIGIHIIIJIKILIMINIycPIQIRI8w9wSITIUIVIWIXIYIZI0I1I2I3Izc5I6I7I!w#w9I!I#I$I%I'I(I)I*I,I-I.Iyb/I$w%w:I;I=I?I@I[I]I^I_I'w$b)w*w+w,w-w.w/w:w;w=w?w@w[w]w^w_w`w{w|w}w~waxbxcxdxexfxzb~IgxhxaJbJcJdJeJfJgJhJAciJjJkJixjxlJmJnJoJpJqJrJsJtJuJvJwJxJyJzJAJBJCJDJEJBcFJGJHJkxlxIJJJKJLJMJNJOJPJQJRJSJCcTJmxnxUJVJWJXJYJZJ0J1J2JIc3J4J5Joxpx6J7J8J9J!J#J$J%J'J(J)J7 *Jqxrx+J,J-J.J/J_ :Jsxtx;J=J?J@J[J]J^JKc_J`J{Juxvx|J}J~JaKbKcKdKeKfKgKhKiKLcjKkKwxxxlKmKnKoKpKqKrKsKtKyxBbAxBxCxQrRrExFxGxHxIxJxKxLxMxNxOxyKzKMcBKCKDKPxQxFKGKHKIKJKKKLKMKNKPKQKRKNcTKUKVKRxSxXKYKZK0K1K2K3K4K5K7K8K9KOc#K$K%KTxUx(K)K*K+K,K-K.K/K:K=K?K@KPc]K^K_KVxWx{K|K}K~KaLbLcLdLeLgLhLiLQckLlLmLXxYxoLpLqLrLsLtLuLvLwLyLzLALRcCLDLELZx0xGLHLILJLKLLLMLNLOLQLRLSLScULVLWL1x2xYLZL0L1L2L3L4L5L6L8L9L!LTc$L%L'L3x4x)L*L+L,L-L.L/L:L;L?L@LZ
1345cdef CUresult cuGraphExecUpdate(CUgraphExec hGraphExec, CUgraph hGraph, CUgraphExecUpdateResultInfo* resultInfo) except ?CUDA_ERROR_NOT_FOUND nogil:
1346 return _driver._cuGraphExecUpdate_v2(hGraphExec, hGraph, resultInfo) 2G 1 2 Lb
1349cdef CUresult cuGraphKernelNodeCopyAttributes(CUgraphNode dst, CUgraphNode src) except ?CUDA_ERROR_NOT_FOUND nogil:
1350 return _driver._cuGraphKernelNodeCopyAttributes(dst, src)
1353cdef CUresult cuGraphKernelNodeGetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, CUkernelNodeAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1354 return _driver._cuGraphKernelNodeGetAttribute(hNode, attr, value_out)
1357cdef CUresult cuGraphKernelNodeSetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, const CUkernelNodeAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1358 return _driver._cuGraphKernelNodeSetAttribute(hNode, attr, value)
1361cdef CUresult cuGraphDebugDotPrint(CUgraph hGraph, const char* path, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1362 return _driver._cuGraphDebugDotPrint(hGraph, path, flags) 2`u{uW
1365cdef CUresult cuUserObjectCreate(CUuserObject* object_out, void* ptr, CUhostFn destroy, unsigned int initialRefcount, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1366 return _driver._cuUserObjectCreate(object_out, ptr, destroy, initialRefcount, flags) 2ObPbpd5 ]bqdrdDbEbFb*bGb/inl|bbece(l)lxd}beefe:l;lyd~bheiecmdmzdackelekmlmAdbcneoesmtmBdccqereAmBmCd^dHbIbJbKb^b_b.bIh_dejQbRb`dfjM P dg0 | } /b`bQ N A B C b 2 ic5j6jVnMejc#j$j2nOe1bQeReygJd* 8c9cMdnbobpb3b/ : ; = qb~iFgdi#ckc+j,j$nWe4bhiii/jSdrbUdVdYe$c5b^j_j`jWdoipi4e5e6e7eqi8e9e!e#esbYdZd$elcckdk:n*eMgNgOgPgmc1d2d,e/enc'c(c)c3docpctbqcrcsctcikjk|n?e6 6b7buc? .c/c4dvc`e{eTg|ewcnkVpho}eub1g2gzi:cxctkukoobf8bdfef4g7d+ =c?c!d9bvbwb#b@ [ ] ^ xb!g#gLi[cycAkBkzojfzcFkGkGolfyb)d*dnf]c$bKkLkMk+dSiTitfufvfwfUixfyfzfAfzb-d.dBfAcTkUkOoGf*g+g,g-gBc:d;dIfLfCc_c`c{c=dDcEcAbFcGcHcIcZk0kZoPf7 %b'bJc_ bdcd?dKc;g=gYiVfLc6k7k8oXfBb[g]g6iddMc$k%k)o0fNc*k+k:o2fOc/k:k^o4fPc@k[kap6fQc`k{khp8fRcalblop!fScflglvp$fTcklllCp'f
1369cdef CUresult cuUserObjectRetain(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1370 return _driver._cuUserObjectRetain(object, count)
1373cdef CUresult cuUserObjectRelease(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1374 return _driver._cuUserObjectRelease(object, count)
1377cdef CUresult cuGraphRetainUserObject(CUgraph graph, CUuserObject object, unsigned int count, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1378 return _driver._cuGraphRetainUserObject(graph, object, count, flags) 2ObPbpd5 ]bqdrdDbEbFb*bGb/inl|bbece(l)lxd}beefe:l;lyd~bheiecmdmzdackelekmlmAdbcneoesmtmBdccqereAmBmCd^dHbIbJbKb^b_b.bIh_dejQbRb`dfjM P dg0 | } /b`bQ N A B C b 2 ic5j6jVnMejc#j$j2nOe1bQeReygJd* 8c9cMdnbobpb3b/ : ; = qb~iFgdi#ckc+j,j$nWe4bhiii/jSdrbUdVdYe$c5b^j_j`jWdoipi4e5e6e7eqi8e9e!e#esbYdZd$elcckdk:n*eMgNgOgPgmc1d2d,e/enc'c(c)c3docpctbqcrcsctcikjk|n?e6 6b7buc? .c/c4dvc`e{eTg|ewcnkVpho}eub1g2gzi:cxctkukoobf8bdfef4g7d+ =c?c!d9bvbwb#b@ [ ] ^ xb!g#gLi[cycAkBkzojfzcFkGkGolfyb)d*dnf]c$bKkLkMk+dSiTitfufvfwfUixfyfzfAfzb-d.dBfAcTkUkOoGf*g+g,g-gBc:d;dIfLfCc_c`c{c=dDcEcAbFcGcHcIcZk0kZoPf7 %b'bJc_ bdcd?dKc;g=gYiVfLc6k7k8oXfBb[g]g6iddMc$k%k)o0fNc*k+k:o2fOc/k:k^o4fPc@k[kap6fQc`k{khp8fRcalblop!fScflglvp$fTcklllCp'f
1381cdef CUresult cuGraphReleaseUserObject(CUgraph graph, CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1382 return _driver._cuGraphReleaseUserObject(graph, object, count)
1385cdef CUresult cuGraphAddNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1386 return _driver._cuGraphAddNode_v2(phGraphNode, hGraph, dependencies, dependencyData, numDependencies, nodeParams) 2c d e f g h i j k l m n o p q r H s t u v w I J K L }x*l+l,l-l=l?l@l[lemfmgmhmmmnmompmumvmwmxmCmDmEmFm4l5lWpXpYpZpHbIbJbKbajG W 4MHsbbWnXnUrZn3nVr5n6nzgAgBgCgNdOdPdQd/ : ; = 7n8n9n!n%n'n)n*n:j;j?j@jZe0e2e3e{j|j~jak4e5e6e7e8e9e!e#e%e'e(e)e;n=n?n@nMgNgOgPg[n]n^n_n`n-e.e;e=eocpcrcsc}n~nboco*c+c,c-c[e]e^e_eUgVgXgYgiojokoloAiBiDiEimopoqosoto5g6g7g8g#d$d%d'd@ [ ] ^ uovowoxoAoBoDoEoHoIoKoLoofpfrfsfNkOkQkRktfufvfwfxfyfzfAfCfDfEfFfPoQoRoSo*g+g,g-gToUoVoWoXoJfKfNfOfDcEcGcHc0o1o3o4o|c}c~cadRfSfTfUfZi0i2i3i9o!o#o$o7i8i!i#i'o*o+o-o.o;o=o@o[o_o`o|o}obpcpepfpipjplpmpppqpsptpwpxpzpApDpEpGpHp
1389cdef CUresult cuGraphNodeSetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1390 return _driver._cuGraphNodeSetParams(hNode, nodeParams) 2bb
1393cdef CUresult cuGraphExecNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1394 return _driver._cuGraphExecNodeSetParams(hGraphExec, hNode, nodeParams) 2bb
1397cdef CUresult cuGraphConditionalHandleCreate(CUgraphConditionalHandle* pHandle_out, CUgraph hGraph, CUcontext ctx, unsigned int defaultLaunchValue, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1398 return _driver._cuGraphConditionalHandleCreate(pHandle_out, hGraph, ctx, defaultLaunchValue, flags) 2c d e f g h i j k l m n o p q r H s t u v w I J K L }x*l+l,l-l=l?l@l[lemfmgmhmmmnmompmumvmwmxmCmDmEmFm4l~x5lWpXpYpZpHbIbJbKbajG W 4M7qWnXnUrZn9q3nVr5n6nzgAgBgCgUeNdOdPdQd/ : ; = ciqbEg~iFgGgdi7n8n#cRdHg#q9n!n$q%n'n)n*n+n:j;j?j@jZe0e2e3e-n{j|j~jak4e5e6e7e8e9e!e#e%e'e(e)e(q;n=n?n@nMgNgOgPg[n]n^n_n`nQg-e.e;e=eocpcrcsc)q}n~nboco*c+c,c-c[e]e^e_euiUgVgXgYgiojokolopkAiBiDiEimo.qpoqosoto5g6g7g8ghf#d$d%d'd@ [ ] ^ Kixb9g!g#g$gLiuovo[c(d%g:qwoxo;qAoBoDoEo=qHoIoKoLoofpfrfsfMoNkOkQkRktfufvfwfxfyfzfAfCfDfEfFf@qPoQoRoSo*g+g,g-gToUoVoWoXo.gJfKfNfOfDcEcGcHc[q0o1o3o4o|c}c~cadRfSfTfUf2kZi0i2i3i9o!o#o$o9k7i8i!i#i'o|q*o+o-o.oar;o=o@o[ocr_o`o|o}oerbpcpepfpgripjplpmpirppqpsptpkrwpxpzpAplrDpEpGpHp
1401cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize) except ?CUDA_ERROR_NOT_FOUND nogil:
1402 return _driver._cuOccupancyMaxActiveBlocksPerMultiprocessor(numBlocks, func, blockSize, dynamicSMemSize) 2dcavbvcvdvevfvgvhvivjvkvlvmvnvovpvqvrv
1405cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1406 return _driver._cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(numBlocks, func, blockSize, dynamicSMemSize, flags)
1409cdef CUresult cuOccupancyMaxPotentialBlockSize(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit) except ?CUDA_ERROR_NOT_FOUND nogil:
1410 return _driver._cuOccupancyMaxPotentialBlockSize(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit) 2%C'C(C)C*C+C,C-C.C/C:C;C=C?C@C[C]C^C_C`C{C
1413cdef CUresult cuOccupancyMaxPotentialBlockSizeWithFlags(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1414 return _driver._cuOccupancyMaxPotentialBlockSizeWithFlags(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit, flags)
1417cdef CUresult cuOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, CUfunction func, int numBlocks, int blockSize) except ?CUDA_ERROR_NOT_FOUND nogil:
1418 return _driver._cuOccupancyAvailableDynamicSMemPerBlock(dynamicSmemSize, func, numBlocks, blockSize) 27C8C9C!C#C$C
1421cdef CUresult cuOccupancyMaxPotentialClusterSize(int* clusterSize, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1422 return _driver._cuOccupancyMaxPotentialClusterSize(clusterSize, func, config)
1425cdef CUresult cuOccupancyMaxActiveClusters(int* numClusters, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1426 return _driver._cuOccupancyMaxActiveClusters(numClusters, func, config)
1429cdef CUresult cuTexRefSetArray(CUtexref hTexRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1430 return _driver._cuTexRefSetArray(hTexRef, hArray, Flags)
1433cdef CUresult cuTexRefSetMipmappedArray(CUtexref hTexRef, CUmipmappedArray hMipmappedArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1434 return _driver._cuTexRefSetMipmappedArray(hTexRef, hMipmappedArray, Flags)
1437cdef CUresult cuTexRefSetAddress(size_t* ByteOffset, CUtexref hTexRef, CUdeviceptr dptr, size_t bytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1438 return _driver._cuTexRefSetAddress_v2(ByteOffset, hTexRef, dptr, bytes)
1441cdef CUresult cuTexRefSetAddress2D(CUtexref hTexRef, const CUDA_ARRAY_DESCRIPTOR* desc, CUdeviceptr dptr, size_t Pitch) except ?CUDA_ERROR_NOT_FOUND nogil:
1442 return _driver._cuTexRefSetAddress2D_v3(hTexRef, desc, dptr, Pitch)
1445cdef CUresult cuTexRefSetFormat(CUtexref hTexRef, CUarray_format fmt, int NumPackedComponents) except ?CUDA_ERROR_NOT_FOUND nogil:
1446 return _driver._cuTexRefSetFormat(hTexRef, fmt, NumPackedComponents)
1449cdef CUresult cuTexRefSetAddressMode(CUtexref hTexRef, int dim, CUaddress_mode am) except ?CUDA_ERROR_NOT_FOUND nogil:
1450 return _driver._cuTexRefSetAddressMode(hTexRef, dim, am)
1453cdef CUresult cuTexRefSetFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1454 return _driver._cuTexRefSetFilterMode(hTexRef, fm)
1457cdef CUresult cuTexRefSetMipmapFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1458 return _driver._cuTexRefSetMipmapFilterMode(hTexRef, fm)
1461cdef CUresult cuTexRefSetMipmapLevelBias(CUtexref hTexRef, float bias) except ?CUDA_ERROR_NOT_FOUND nogil:
1462 return _driver._cuTexRefSetMipmapLevelBias(hTexRef, bias)
1465cdef CUresult cuTexRefSetMipmapLevelClamp(CUtexref hTexRef, float minMipmapLevelClamp, float maxMipmapLevelClamp) except ?CUDA_ERROR_NOT_FOUND nogil:
1466 return _driver._cuTexRefSetMipmapLevelClamp(hTexRef, minMipmapLevelClamp, maxMipmapLevelClamp)
1469cdef CUresult cuTexRefSetMaxAnisotropy(CUtexref hTexRef, unsigned int maxAniso) except ?CUDA_ERROR_NOT_FOUND nogil:
1470 return _driver._cuTexRefSetMaxAnisotropy(hTexRef, maxAniso)
1473cdef CUresult cuTexRefSetBorderColor(CUtexref hTexRef, float* pBorderColor) except ?CUDA_ERROR_NOT_FOUND nogil:
1474 return _driver._cuTexRefSetBorderColor(hTexRef, pBorderColor)
1477cdef CUresult cuTexRefSetFlags(CUtexref hTexRef, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1478 return _driver._cuTexRefSetFlags(hTexRef, Flags)
1481cdef CUresult cuTexRefGetAddress(CUdeviceptr* pdptr, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1482 return _driver._cuTexRefGetAddress_v2(pdptr, hTexRef)
1485cdef CUresult cuTexRefGetArray(CUarray* phArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1486 return _driver._cuTexRefGetArray(phArray, hTexRef)
1489cdef CUresult cuTexRefGetMipmappedArray(CUmipmappedArray* phMipmappedArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1490 return _driver._cuTexRefGetMipmappedArray(phMipmappedArray, hTexRef)
1493cdef CUresult cuTexRefGetAddressMode(CUaddress_mode* pam, CUtexref hTexRef, int dim) except ?CUDA_ERROR_NOT_FOUND nogil:
1494 return _driver._cuTexRefGetAddressMode(pam, hTexRef, dim)
1497cdef CUresult cuTexRefGetFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1498 return _driver._cuTexRefGetFilterMode(pfm, hTexRef)
1501cdef CUresult cuTexRefGetFormat(CUarray_format* pFormat, int* pNumChannels, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1502 return _driver._cuTexRefGetFormat(pFormat, pNumChannels, hTexRef)
1505cdef CUresult cuTexRefGetMipmapFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1506 return _driver._cuTexRefGetMipmapFilterMode(pfm, hTexRef)
1509cdef CUresult cuTexRefGetMipmapLevelBias(float* pbias, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1510 return _driver._cuTexRefGetMipmapLevelBias(pbias, hTexRef)
1513cdef CUresult cuTexRefGetMipmapLevelClamp(float* pminMipmapLevelClamp, float* pmaxMipmapLevelClamp, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1514 return _driver._cuTexRefGetMipmapLevelClamp(pminMipmapLevelClamp, pmaxMipmapLevelClamp, hTexRef)
1517cdef CUresult cuTexRefGetMaxAnisotropy(int* pmaxAniso, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1518 return _driver._cuTexRefGetMaxAnisotropy(pmaxAniso, hTexRef)
1521cdef CUresult cuTexRefGetBorderColor(float* pBorderColor, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1522 return _driver._cuTexRefGetBorderColor(pBorderColor, hTexRef)
1525cdef CUresult cuTexRefGetFlags(unsigned int* pFlags, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1526 return _driver._cuTexRefGetFlags(pFlags, hTexRef)
1529cdef CUresult cuTexRefCreate(CUtexref* pTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1530 return _driver._cuTexRefCreate(pTexRef)
1533cdef CUresult cuTexRefDestroy(CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1534 return _driver._cuTexRefDestroy(hTexRef)
1537cdef CUresult cuSurfRefSetArray(CUsurfref hSurfRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1538 return _driver._cuSurfRefSetArray(hSurfRef, hArray, Flags)
1541cdef CUresult cuSurfRefGetArray(CUarray* phArray, CUsurfref hSurfRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1542 return _driver._cuSurfRefGetArray(phArray, hSurfRef)
1545cdef 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:
1546 return _driver._cuTexObjectCreate(pTexObject, pResDesc, pTexDesc, pResViewDesc) 2)r.r|g/r}g:rLh
1549cdef CUresult cuTexObjectDestroy(CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1550 return _driver._cuTexObjectDestroy(texObject) 2)r.r|g/r}g:rLh
1553cdef CUresult cuTexObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1554 return _driver._cuTexObjectGetResourceDesc(pResDesc, texObject)
1557cdef CUresult cuTexObjectGetTextureDesc(CUDA_TEXTURE_DESC* pTexDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1558 return _driver._cuTexObjectGetTextureDesc(pTexDesc, texObject)
1561cdef CUresult cuTexObjectGetResourceViewDesc(CUDA_RESOURCE_VIEW_DESC* pResViewDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1562 return _driver._cuTexObjectGetResourceViewDesc(pResViewDesc, texObject)
1565cdef CUresult cuSurfObjectCreate(CUsurfObject* pSurfObject, const CUDA_RESOURCE_DESC* pResDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
1566 return _driver._cuSurfObjectCreate(pSurfObject, pResDesc) 2,r-rLh
1569cdef CUresult cuSurfObjectDestroy(CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1570 return _driver._cuSurfObjectDestroy(surfObject) 2,r-rLh
1573cdef CUresult cuSurfObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1574 return _driver._cuSurfObjectGetResourceDesc(pResDesc, surfObject)
1577cdef 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:
1578 return _driver._cuTensorMapEncodeTiled(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, boxDim, elementStrides, interleave, swizzle, l2Promotion, oobFill)
1581cdef 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:
1582 return _driver._cuTensorMapEncodeIm2col(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCorner, pixelBoxUpperCorner, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, swizzle, l2Promotion, oobFill)
1585cdef 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:
1586 return _driver._cuTensorMapEncodeIm2colWide(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCornerWidth, pixelBoxUpperCornerWidth, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, mode, swizzle, l2Promotion, oobFill)
1589cdef CUresult cuTensorMapReplaceAddress(CUtensorMap* tensorMap, void* globalAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1590 return _driver._cuTensorMapReplaceAddress(tensorMap, globalAddress)
1593cdef CUresult cuDeviceCanAccessPeer(int* canAccessPeer, CUdevice dev, CUdevice peerDev) except ?CUDA_ERROR_NOT_FOUND nogil:
1594 return _driver._cuDeviceCanAccessPeer(canAccessPeer, dev, peerDev)
1597cdef CUresult cuCtxEnablePeerAccess(CUcontext peerContext, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1598 return _driver._cuCtxEnablePeerAccess(peerContext, Flags)
1601cdef CUresult cuCtxDisablePeerAccess(CUcontext peerContext) except ?CUDA_ERROR_NOT_FOUND nogil:
1602 return _driver._cuCtxDisablePeerAccess(peerContext)
1605cdef CUresult cuDeviceGetP2PAttribute(int* value, CUdevice_P2PAttribute attrib, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil:
1606 return _driver._cuDeviceGetP2PAttribute(value, attrib, srcDevice, dstDevice)
1609cdef CUresult cuGraphicsUnregisterResource(CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1610 return _driver._cuGraphicsUnregisterResource(resource) 2~gahbhSjG1H1I1J1K1chdheh{iL1fhghM1hh
1613cdef CUresult cuGraphicsSubResourceGetMappedArray(CUarray* pArray, CUgraphicsResource resource, unsigned int arrayIndex, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil:
1614 return _driver._cuGraphicsSubResourceGetMappedArray(pArray, resource, arrayIndex, mipLevel)
1617cdef CUresult cuGraphicsResourceGetMappedMipmappedArray(CUmipmappedArray* pMipmappedArray, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1618 return _driver._cuGraphicsResourceGetMappedMipmappedArray(pMipmappedArray, resource)
1621cdef CUresult cuGraphicsResourceGetMappedPointer(CUdeviceptr* pDevPtr, size_t* pSize, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1622 return _driver._cuGraphicsResourceGetMappedPointer_v2(pDevPtr, pSize, resource) 2~gUpahbhchdheh{ifhghhhFl
1625cdef CUresult cuGraphicsResourceSetMapFlags(CUgraphicsResource resource, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1626 return _driver._cuGraphicsResourceSetMapFlags_v2(resource, flags)
1629cdef CUresult cuGraphicsMapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1630 return _driver._cuGraphicsMapResources(count, resources, hStream) 2~gUpahbhchdheh{ifhghhhFl
1633cdef CUresult cuGraphicsUnmapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1634 return _driver._cuGraphicsUnmapResources(count, resources, hStream) 2~gahbhchdheh{ifhghhhFl
1637cdef CUresult cuGetProcAddress(const char* symbol, void** pfn, int cudaVersion, cuuint64_t flags, CUdriverProcAddressQueryResult* symbolStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
1638 return _driver._cuGetProcAddress_v2(symbol, pfn, cudaVersion, flags, symbolStatus)
1641cdef CUresult cuCoredumpGetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1642 return _driver._cuCoredumpGetAttribute(attrib, value, size)
1645cdef CUresult cuCoredumpGetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1646 return _driver._cuCoredumpGetAttributeGlobal(attrib, value, size) 2N1
1649cdef CUresult cuCoredumpSetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1650 return _driver._cuCoredumpSetAttribute(attrib, value, size)
1653cdef CUresult cuCoredumpSetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1654 return _driver._cuCoredumpSetAttributeGlobal(attrib, value, size) 2N1
1657cdef CUresult cuGetExportTable(const void** ppExportTable, const CUuuid* pExportTableId) except ?CUDA_ERROR_NOT_FOUND nogil:
1658 return _driver._cuGetExportTable(ppExportTable, pExportTableId)
1661cdef CUresult cuGreenCtxCreate(CUgreenCtx* phCtx, CUdevResourceDesc desc, CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1662 return _driver._cuGreenCtxCreate(phCtx, desc, dev, flags) 2HlTjUjweX Y VjWjXjYjZj0j
1665cdef CUresult cuGreenCtxDestroy(CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1666 return _driver._cuGreenCtxDestroy(hCtx) 2HlpFqFrFX Y sFtFuFvFwFxF
1669cdef CUresult cuCtxFromGreenCtx(CUcontext* pContext, CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1670 return _driver._cuCtxFromGreenCtx(pContext, hCtx) 2HlTjUjweX Y VjWjXjYjZj0j
1673cdef CUresult cuDeviceGetDevResource(CUdevice device, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1674 return _driver._cuDeviceGetDevResource(device, resource, type) 2O1P1iATjUjweXmYmVjWjXjYjZj0jjAkAlAmAnAoApAqArAsAtAuAvAwAxAyAzAAA
1677cdef CUresult cuCtxGetDevResource(CUcontext hCtx, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1678 return _driver._cuCtxGetDevResource(hCtx, resource, type)
1681cdef CUresult cuGreenCtxGetDevResource(CUgreenCtx hCtx, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1682 return _driver._cuGreenCtxGetDevResource(hCtx, resource, type) 2Hl?5By
1685cdef CUresult cuDevSmResourceSplitByCount(CUdevResource* result, unsigned int* nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, unsigned int minCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1686 return _driver._cuDevSmResourceSplitByCount(result, nbGroups, input, remainder, flags, minCount) 2P1
1689cdef CUresult cuDevResourceGenerateDesc(CUdevResourceDesc* phDesc, CUdevResource* resources, unsigned int nbResources) except ?CUDA_ERROR_NOT_FOUND nogil:
1690 return _driver._cuDevResourceGenerateDesc(phDesc, resources, nbResources) 2HlTjUjweX Y VjWjXjYjZj0j
1693cdef CUresult cuGreenCtxRecordEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1694 return _driver._cuGreenCtxRecordEvent(hCtx, hEvent)
1697cdef CUresult cuGreenCtxWaitEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1698 return _driver._cuGreenCtxWaitEvent(hCtx, hEvent)
1701cdef CUresult cuStreamGetGreenCtx(CUstream hStream, CUgreenCtx* phCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1702 return _driver._cuStreamGetGreenCtx(hStream, phCtx)
1705cdef CUresult cuGreenCtxStreamCreate(CUstream* phStream, CUgreenCtx greenCtx, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil:
1706 return _driver._cuGreenCtxStreamCreate(phStream, greenCtx, flags, priority) 2ByMbX Y c1VMkj
1709cdef CUresult cuLogsRegisterCallback(CUlogsCallback callbackFunc, void* userData, CUlogsCallbackHandle* callback_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1710 return _driver._cuLogsRegisterCallback(callbackFunc, userData, callback_out)
1713cdef CUresult cuLogsUnregisterCallback(CUlogsCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
1714 return _driver._cuLogsUnregisterCallback(callback)
1717cdef CUresult cuLogsCurrent(CUlogIterator* iterator_out, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1718 return _driver._cuLogsCurrent(iterator_out, flags)
1721cdef CUresult cuLogsDumpToFile(CUlogIterator* iterator, const char* pathToFile, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1722 return _driver._cuLogsDumpToFile(iterator, pathToFile, flags)
1725cdef CUresult cuLogsDumpToMemory(CUlogIterator* iterator, char* buffer, size_t* size, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1726 return _driver._cuLogsDumpToMemory(iterator, buffer, size, flags)
1729cdef CUresult cuCheckpointProcessGetRestoreThreadId(int pid, int* tid) except ?CUDA_ERROR_NOT_FOUND nogil:
1730 return _driver._cuCheckpointProcessGetRestoreThreadId(pid, tid)
1733cdef CUresult cuCheckpointProcessGetState(int pid, CUprocessState* state) except ?CUDA_ERROR_NOT_FOUND nogil:
1734 return _driver._cuCheckpointProcessGetState(pid, state) 2@5
1737cdef CUresult cuCheckpointProcessLock(int pid, CUcheckpointLockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1738 return _driver._cuCheckpointProcessLock(pid, args)
1741cdef CUresult cuCheckpointProcessCheckpoint(int pid, CUcheckpointCheckpointArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1742 return _driver._cuCheckpointProcessCheckpoint(pid, args)
1745cdef CUresult cuCheckpointProcessRestore(int pid, CUcheckpointRestoreArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1746 return _driver._cuCheckpointProcessRestore(pid, args)
1749cdef CUresult cuCheckpointProcessUnlock(int pid, CUcheckpointUnlockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1750 return _driver._cuCheckpointProcessUnlock(pid, args)
1753cdef CUresult cuGraphicsEGLRegisterImage(CUgraphicsResource* pCudaResource, EGLImageKHR image, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1754 return _driver._cuGraphicsEGLRegisterImage(pCudaResource, image, flags)
1757cdef CUresult cuEGLStreamConsumerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream) except ?CUDA_ERROR_NOT_FOUND nogil:
1758 return _driver._cuEGLStreamConsumerConnect(conn, stream)
1761cdef CUresult cuEGLStreamConsumerConnectWithFlags(CUeglStreamConnection* conn, EGLStreamKHR stream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1762 return _driver._cuEGLStreamConsumerConnectWithFlags(conn, stream, flags)
1765cdef CUresult cuEGLStreamConsumerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1766 return _driver._cuEGLStreamConsumerDisconnect(conn)
1769cdef CUresult cuEGLStreamConsumerAcquireFrame(CUeglStreamConnection* conn, CUgraphicsResource* pCudaResource, CUstream* pStream, unsigned int timeout) except ?CUDA_ERROR_NOT_FOUND nogil:
1770 return _driver._cuEGLStreamConsumerAcquireFrame(conn, pCudaResource, pStream, timeout)
1773cdef CUresult cuEGLStreamConsumerReleaseFrame(CUeglStreamConnection* conn, CUgraphicsResource pCudaResource, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1774 return _driver._cuEGLStreamConsumerReleaseFrame(conn, pCudaResource, pStream)
1777cdef CUresult cuEGLStreamProducerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream, EGLint width, EGLint height) except ?CUDA_ERROR_NOT_FOUND nogil:
1778 return _driver._cuEGLStreamProducerConnect(conn, stream, width, height)
1781cdef CUresult cuEGLStreamProducerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1782 return _driver._cuEGLStreamProducerDisconnect(conn)
1785cdef CUresult cuEGLStreamProducerPresentFrame(CUeglStreamConnection* conn, CUeglFrame eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1786 return _driver._cuEGLStreamProducerPresentFrame(conn, eglframe, pStream)
1789cdef CUresult cuEGLStreamProducerReturnFrame(CUeglStreamConnection* conn, CUeglFrame* eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1790 return _driver._cuEGLStreamProducerReturnFrame(conn, eglframe, pStream)
1793cdef CUresult cuGraphicsResourceGetMappedEglFrame(CUeglFrame* eglFrame, CUgraphicsResource resource, unsigned int index, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil:
1794 return _driver._cuGraphicsResourceGetMappedEglFrame(eglFrame, resource, index, mipLevel)
1797cdef CUresult cuEventCreateFromEGLSync(CUevent* phEvent, EGLSyncKHR eglSync, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1798 return _driver._cuEventCreateFromEGLSync(phEvent, eglSync, flags)
1801cdef CUresult cuGraphicsGLRegisterBuffer(CUgraphicsResource* pCudaResource, GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1802 return _driver._cuGraphicsGLRegisterBuffer(pCudaResource, buffer, Flags) 2~gUpahbhSjG1H1I1J1K1chdheh{iL1fhghM1hhFl}M~MaNbN
1805cdef CUresult cuGraphicsGLRegisterImage(CUgraphicsResource* pCudaResource, GLuint image, GLenum target, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1806 return _driver._cuGraphicsGLRegisterImage(pCudaResource, image, target, Flags) 2|M
1809cdef CUresult cuGLGetDevices(unsigned int* pCudaDeviceCount, CUdevice* pCudaDevices, unsigned int cudaDeviceCount, CUGLDeviceList deviceList) except ?CUDA_ERROR_NOT_FOUND nogil:
1810 return _driver._cuGLGetDevices_v2(pCudaDeviceCount, pCudaDevices, cudaDeviceCount, deviceList)
1813cdef CUresult cuGLCtxCreate(CUcontext* pCtx, unsigned int Flags, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
1814 return _driver._cuGLCtxCreate_v2(pCtx, Flags, device)
1817cdef CUresult cuGLInit() except ?CUDA_ERROR_NOT_FOUND nogil:
1818 return _driver._cuGLInit()
1821cdef CUresult cuGLRegisterBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1822 return _driver._cuGLRegisterBufferObject(buffer)
1825cdef CUresult cuGLMapBufferObject(CUdeviceptr* dptr, size_t* size, GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1826 return _driver._cuGLMapBufferObject_v2(dptr, size, buffer)
1829cdef CUresult cuGLUnmapBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1830 return _driver._cuGLUnmapBufferObject(buffer)
1833cdef CUresult cuGLUnregisterBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1834 return _driver._cuGLUnregisterBufferObject(buffer)
1837cdef CUresult cuGLSetBufferObjectMapFlags(GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1838 return _driver._cuGLSetBufferObjectMapFlags(buffer, Flags)
1841cdef CUresult cuGLMapBufferObjectAsync(CUdeviceptr* dptr, size_t* size, GLuint buffer, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1842 return _driver._cuGLMapBufferObjectAsync_v2(dptr, size, buffer, hStream)
1845cdef CUresult cuGLUnmapBufferObjectAsync(GLuint buffer, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1846 return _driver._cuGLUnmapBufferObjectAsync(buffer, hStream)
1849cdef CUresult cuProfilerInitialize(const char* configFile, const char* outputFile, CUoutput_mode outputMode) except ?CUDA_ERROR_NOT_FOUND nogil:
1850 return _driver._cuProfilerInitialize(configFile, outputFile, outputMode)
1853cdef CUresult cuProfilerStart() except ?CUDA_ERROR_NOT_FOUND nogil:
1854 return _driver._cuProfilerStart() 2Q1
1857cdef CUresult cuProfilerStop() except ?CUDA_ERROR_NOT_FOUND nogil:
1858 return _driver._cuProfilerStop() 2Q1
1861cdef CUresult cuVDPAUGetDevice(CUdevice* pDevice, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1862 return _driver._cuVDPAUGetDevice(pDevice, vdpDevice, vdpGetProcAddress)
1865cdef CUresult cuVDPAUCtxCreate(CUcontext* pCtx, unsigned int flags, CUdevice device, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1866 return _driver._cuVDPAUCtxCreate_v2(pCtx, flags, device, vdpDevice, vdpGetProcAddress)
1869cdef CUresult cuGraphicsVDPAURegisterVideoSurface(CUgraphicsResource* pCudaResource, VdpVideoSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1870 return _driver._cuGraphicsVDPAURegisterVideoSurface(pCudaResource, vdpSurface, flags)
1873cdef CUresult cuGraphicsVDPAURegisterOutputSurface(CUgraphicsResource* pCudaResource, VdpOutputSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1874 return _driver._cuGraphicsVDPAURegisterOutputSurface(pCudaResource, vdpSurface, flags)
1877cdef CUresult cuDeviceGetHostAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
1878 return _driver._cuDeviceGetHostAtomicCapabilities(capabilities, operations, count, dev)
1881cdef CUresult cuCtxGetDevice_v2(CUdevice* device, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1882 return _driver._cuCtxGetDevice_v2(device, ctx)
1885cdef CUresult cuCtxSynchronize_v2(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1886 return _driver._cuCtxSynchronize_v2(ctx)
1889cdef 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:
1890 return _driver._cuMemcpyBatchAsync_v2(dsts, srcs, sizes, count, attrs, attrsIdxs, numAttrs, hStream)
1893cdef CUresult cuMemcpy3DBatchAsync(size_t numOps, CUDA_MEMCPY3D_BATCH_OP* opList, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1894 return _driver._cuMemcpy3DBatchAsync_v2(numOps, opList, flags, hStream)
1897cdef CUresult cuMemGetDefaultMemPool(CUmemoryPool* pool_out, CUmemLocation* location, CUmemAllocationType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1898 return _driver._cuMemGetDefaultMemPool(pool_out, location, type)
1901cdef CUresult cuMemGetMemPool(CUmemoryPool* pool, CUmemLocation* location, CUmemAllocationType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1902 return _driver._cuMemGetMemPool(pool, location, type) 2Jq8lRqTmLjvdUmMjVmNjUqVqWqXqYqZq0qpl3c|uql}u(h)h*h~umbDdrl;hYC5cZCrg0Csg1Ctg2Cug3C6c4Cvg5Cxg7cKesl
1905cdef CUresult cuMemSetMemPool(CUmemLocation* location, CUmemAllocationType type, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
1906 return _driver._cuMemSetMemPool(location, type, pool)
1909cdef 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:
1910 return _driver._cuMemPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 2igaejgkg
1913cdef CUresult cuMemDiscardBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1914 return _driver._cuMemDiscardBatchAsync(dptrs, sizes, count, flags, hStream) 2igWlXl
1917cdef 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:
1918 return _driver._cuMemDiscardAndPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 2aevd
1921cdef CUresult cuDeviceGetP2PAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil:
1922 return _driver._cuDeviceGetP2PAtomicCapabilities(capabilities, operations, count, srcDevice, dstDevice)
1925cdef CUresult cuGreenCtxGetId(CUgreenCtx greenCtx, unsigned long long* greenCtxId) except ?CUDA_ERROR_NOT_FOUND nogil:
1926 return _driver._cuGreenCtxGetId(greenCtx, greenCtxId)
1929cdef 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:
1930 return _driver._cuMulticastBindMem_v2(mcHandle, dev, mcOffset, memHandle, memOffset, size, flags)
1933cdef 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:
1934 return _driver._cuMulticastBindAddr_v2(mcHandle, dev, mcOffset, memptr, size, flags)
1937cdef CUresult cuGraphNodeGetContainingGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1938 return _driver._cuGraphNodeGetContainingGraph(hNode, phGraph) 2Hs
1941cdef CUresult cuGraphNodeGetLocalId(CUgraphNode hNode, unsigned int* nodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
1942 return _driver._cuGraphNodeGetLocalId(hNode, nodeId) 2Qy
1945cdef CUresult cuGraphNodeGetToolsId(CUgraphNode hNode, unsigned long long* toolsNodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
1946 return _driver._cuGraphNodeGetToolsId(hNode, toolsNodeId) 2Ry
1949cdef CUresult cuGraphGetId(CUgraph hGraph, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1950 return _driver._cuGraphGetId(hGraph, graphId) 25M
1953cdef CUresult cuGraphExecGetId(CUgraphExec hGraphExec, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1954 return _driver._cuGraphExecGetId(hGraphExec, graphId) 2lj
1957cdef 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:
1958 return _driver._cuDevSmResourceSplit(result, nbGroups, input, remainder, flags, groupParams) 2O1HlTjUjweX Y VjWjXjYjZj0j[5]5^5_5`5{5|5
1961cdef CUresult cuStreamGetDevResource(CUstream hStream, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1962 return _driver._cuStreamGetDevResource(hStream, resource, type) 22M
1965cdef CUresult cuKernelGetParamCount(CUkernel kernel, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1966 return _driver._cuKernelGetParamCount(kernel, paramCount)
1969cdef CUresult cuMemcpyWithAttributesAsync(CUdeviceptr dst, CUdeviceptr src, size_t size, CUmemcpyAttributes* attr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1970 return _driver._cuMemcpyWithAttributesAsync(dst, src, size, attr, hStream)
1973cdef CUresult cuMemcpy3DWithAttributesAsync(CUDA_MEMCPY3D_BATCH_OP* op, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1974 return _driver._cuMemcpy3DWithAttributesAsync(op, flags, hStream)
1977cdef CUresult cuStreamBeginCaptureToCig(CUstream hStream, CUstreamCigCaptureParams* streamCigCaptureParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1978 return _driver._cuStreamBeginCaptureToCig(hStream, streamCigCaptureParams)
1981cdef CUresult cuStreamEndCaptureToCig(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1982 return _driver._cuStreamEndCaptureToCig(hStream)
1985cdef CUresult cuFuncGetParamCount(CUfunction func, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1986 return _driver._cuFuncGetParamCount(func, paramCount)
1989cdef CUresult cuLaunchHostFunc_v2(CUstream hStream, CUhostFn fn, void* userData, unsigned int syncMode) except ?CUDA_ERROR_NOT_FOUND nogil:
1990 return _driver._cuLaunchHostFunc_v2(hStream, fn, userData, syncMode)
1993cdef CUresult cuGraphNodeGetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1994 return _driver._cuGraphNodeGetParams(hNode, nodeParams) 2aj
1997cdef CUresult cuCoredumpRegisterStartCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
1998 return _driver._cuCoredumpRegisterStartCallback(callback, userData, callbackOut)
2001cdef CUresult cuCoredumpRegisterCompleteCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
2002 return _driver._cuCoredumpRegisterCompleteCallback(callback, userData, callbackOut)
2005cdef CUresult cuCoredumpDeregisterStartCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
2006 return _driver._cuCoredumpDeregisterStartCallback(callback)
2009cdef CUresult cuCoredumpDeregisterCompleteCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
2010 return _driver._cuCoredumpDeregisterCompleteCallback(callback)
2013cdef CUresult cuLogicalEndpointIdReserve(CUlogicalEndpointId* baseLeId, cuuint32_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
2014 return _driver._cuLogicalEndpointIdReserve(baseLeId, count)
2017cdef CUresult cuLogicalEndpointIdRelease(CUlogicalEndpointId baseLeId, cuuint32_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
2018 return _driver._cuLogicalEndpointIdRelease(baseLeId, count)
2021cdef CUresult cuLogicalEndpointCreate(CUlogicalEndpointId leId, const CUlogicalEndpointProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
2022 return _driver._cuLogicalEndpointCreate(leId, prop)
2025cdef CUresult cuLogicalEndpointAddDevice(CUlogicalEndpointId leId, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
2026 return _driver._cuLogicalEndpointAddDevice(leId, dev)
2029cdef CUresult cuLogicalEndpointDestroy(CUlogicalEndpointId leId) except ?CUDA_ERROR_NOT_FOUND nogil:
2030 return _driver._cuLogicalEndpointDestroy(leId)
2033cdef CUresult cuLogicalEndpointBindAddr(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, void* ptr, cuuint64_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
2034 return _driver._cuLogicalEndpointBindAddr(leId, dev, offset, ptr, size, flags)
2037cdef CUresult cuLogicalEndpointBindMem(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, CUmemGenericAllocationHandle memHandle, cuuint64_t memOffset, cuuint64_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
2038 return _driver._cuLogicalEndpointBindMem(leId, dev, offset, memHandle, memOffset, size, flags)
2041cdef CUresult cuLogicalEndpointUnbind(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, cuuint64_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
2042 return _driver._cuLogicalEndpointUnbind(leId, dev, offset, size)
2045cdef CUresult cuLogicalEndpointExport(void* handle, CUlogicalEndpointId leId, CUlogicalEndpointIpcHandleType handleType) except ?CUDA_ERROR_NOT_FOUND nogil:
2046 return _driver._cuLogicalEndpointExport(handle, leId, handleType)
2049cdef CUresult cuLogicalEndpointImport(CUlogicalEndpointId leId, const void* handle, CUlogicalEndpointIpcHandleType handleType) except ?CUDA_ERROR_NOT_FOUND nogil:
2050 return _driver._cuLogicalEndpointImport(leId, handle, handleType)
2053cdef CUresult cuLogicalEndpointGetLimits(cuuint64_t* bindAlignment, cuuint64_t* maxSize, const CUlogicalEndpointProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
2054 return _driver._cuLogicalEndpointGetLimits(bindAlignment, maxSize, prop)
2057cdef CUresult cuLogicalEndpointQuery(CUlogicalEndpointId leId, cuuint32_t count, int* queryStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
2058 return _driver._cuLogicalEndpointQuery(leId, count, queryStatus)
2061cdef CUresult cuStreamBeginRecaptureToGraph(CUstream hStream, CUstreamCaptureMode mode, CUgraph hGraph, CUgraphRecaptureCallback callbackFunc, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil:
2062 return _driver._cuStreamBeginRecaptureToGraph(hStream, mode, hGraph, callbackFunc, userData)