Coverage for cuda/bindings/cydriver.pyx: 68.50%
1035 statements
« prev ^ index » next coverage.py v7.15.2, created at 2026-07-29 01:38 +0000
« prev ^ index » next coverage.py v7.15.2, created at 2026-07-29 01:38 +0000
1# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved.
2#
3# SPDX-License-Identifier: Apache-2.0
4#
5# This code was automatically generated across versions from 12.9.0 to 13.3.0. Do not modify it directly.
7# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=5b828e2ee0de9b245c71a6ba9361656ab10f7564caa7e3d9c162b2c6a07fb3df
8from ._internal cimport driver as _driver
10cdef CUresult cuGetErrorString(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil:
11 return _driver._cuGetErrorString(error, pStr) 2IORAJO
14cdef CUresult cuGetErrorName(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil:
15 return _driver._cuGetErrorName(error, pStr) 2ku9mlu!m#m7cB $mIORAJO55KOLOMO8cmi]j
18cdef CUresult cuInit(unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
19 return _driver._cuInit(Flags) 2a SATAUAVAWAXAYAZAni0Amu1A2A3A4A5A6A7A8A9A!A#A$A%A65'A(A)A*A+A,AnuoupuqurusutuuuvuwuxuyuzuAuBuCu'rDuEuFuGuHuIuJuKuLuMuNu-A.A/A:A;A=A?A@A[A]A^A_A`A{A|A}A~AaB
22cdef CUresult cuDriverGetVersion(int* driverVersion) except ?CUDA_ERROR_NOT_FOUND nogil:
23 return _driver._cuDriverGetVersion(driverVersion) 2a 758595!5#5$5
26cdef CUresult cuDeviceGet(CUdevice* device, int ordinal) except ?CUDA_ERROR_NOT_FOUND nogil:
27 return _driver._cuDeviceGet(device, ordinal) 2SATAUAVAWAXAYAZA0A1A2A3A4A5A6A7A8A9A!A#A$A%A'A(A)ARA*A+A,AnuoupuqurusutuuuvuwuxuyuzuAuBuCu'rDuEuFuGuHuIuJuKuLuMuNu-A.A/A:A;A=A?A@A[A]A^A_A`A{A|A}A~AaB
30cdef CUresult cuDeviceGetCount(int* count) except ?CUDA_ERROR_NOT_FOUND nogil:
31 return _driver._cuDeviceGetCount(count) 2a OuNOOOPOQOROSOTOUOVOWOXOYOZO0O1O2O3O4O5O6O7O8O9O!O#O$O%O'O(O)O*O+O,O-O.O/O:O;O=O?O@O[O]O^O_O`O{O|O}O~OaPbPcPdPePfPbBcBdBeBgPfBgBhBiBjB%m^j'mkB_j(m)mlBmBnBoBpBhPqBrBsBtBuBvBwBxByBzBABBBCBDBEBFBGBHBIBJBKBLBMBNBOBPBQBRBSBTBUBVBWBXB*m+m`b`jZe0e{j,m-m.m/m)d1eoipiqiri:m;m=m?m{b|j2e3e}j@m[m]m^m*d4esitiuivi_m`m{m~j|mYBak}m~manbkbnckcndnenfn|bdk5e6eekgnhninjn+d7ewixiyiziknlnmnnn}bfk8e9egkonpnqnrn,d!eAiBiCiDisntnunvn~bhk#e$eikwnxnynzn-d%eEiFiGiHiAnBnCnDnacjk'e(ekkEnFnGnHn.d)eIiJiKiLiInJnKnlkLnmkMnNnOnnkPnokQnRn*eiPSnpkTnqkUnVnjPkPlPmPnPoPpPqPrPsPtPuPvPwPxPyPzPAPBPCPDPEPFPGPHPIPJPKPLPMPNPOPPPQPRPSPTPUPVPWPXPYPZP0P1P2P3P4P5P6P7P8P9P!P#P$P%P'P(P)P*P+P,P-P.P/P:P;P=P?P@P[P]P^P_P`P{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQqQrQsQtQB uQvQZB0B1B2B3B4B5B6B7B8B9B!B#B$B%B'B(B)B*B+B,B-B.BwQ/BxQyQzQAQBQCQDQEQFQGQ(r)rHQPu*rWn+r,r-r.r/r:r;rIQXnrkQuYnskZntkRu=r?r@r[r]r^r_r`r{rJQ0n|ruk}r1n~r`cvkasbs2ncswkds3nesxkfs+e4ngs,eykhs5niszkjsH 6nAkSuTuUuVuWuXuYuZu0u1u2u7n8n.gBk9nksCkls!nms#nns$nos%nps'nqs(nrs)nss*nts+nus,nvs-nws.nxsDkysEkzsFkAsGkBsHkCsIkDsJkEsKkFsLkGsMkHsNkIsOkJsKs/nPk:nniMi;nQkbc=nRkKQLQMQJb?nKbSkob3ucc4udc@necTk-e[nNiUk.e]nOiVkLb5uMb6uNb7uOb8uPb9uQb!umuNQOQPQQQRQSQTQUQVQWQ#u$u%u'u(u)u*u+u,u-u.u/u:u;u{c+ |c^nXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q:BWkXk/e_n`nYkZk0k!Q1k2k3k;B=B?B@B[B]B^B_B`B{B|B}B~BaCbCcCdCeCfCgChC#Q:e}c~cadbdcd=u?u@u[u]u^u_u`u{u|u}u~uavbvcvdvevfvgvhvivjvkvlvmvnvovpvqvrvsvtvuvvvwvxv4kLsyvzvAvBvCvDvEvFvGvHvIvJvKvLvMvNvOvPvQvRvSvTvUvVvWvXvYvZv0v1v2v3v4v5v6v7v8v9v!v#v$v%v'v(v)v*v+v/g;eiCjCfc$Q,v%QddPi'QQi(QRi)QRb/d*QkCSi+Q=e,Q?e9cTi@eUi[eVi]e5k^e_e!cWi:g;g-Qed.Q=g?g/Q@g:Q[g;Qfd=Q]gXi`e:d#c?QYi@Q{eZi[Q|e0i}e1i]Q~e;d$c2iaf^g^Q_g_Q3ibfgd`Q=d{Q6k{n`g|Qgc%c?d|n}Q4i5i~QaRhcbRcRdReRfRgRhRiRjRkRlRmRnRoR}n~npRaoqRbocodorReomisRtRuRvRwRxRyRzRARBRfogohoio-v.v/v:v;v=v?v@v[vCRDRjokolomonooopoqorosotouovowoxoyozoAoBoCoDoEoFoGoHoIoJoKoLoMoNoOoPoQoRoSoToUoVoWoXoYoZo0o1o2o3o4o5o6o7o8o9o!o#o$o%o'o(o)o*o+o,o-o.o/o]v:o^v;o_vlC=o`v?o7kicMsERFR8kmC9k!k#knC@o[o]o^ocfdf6iNsoC{v_o`o$k{o|v|o%kjcOsGRpC'kqC(k)k*krC}o~oapbpefff7iPssC}vcpdpSbgfhf+k{g|g}g@dif8i~gahjf; kf[dhdid]d9i^d_d`dlfkc,klcjdbh!i{d|dpbqbTb| } ~ ab#irbchdhehfh$iepfpkd}dghQsgphpip-kmcRs.k/k:k;ktCjpkplpmpmfHRnf%iSsuCnpop=k'iUbppvC(i~v)i*i+iaw?k@k[k]k~dwCaehhqpbwTs^k_k`ksbbece,iofpfqfldrfihsftf{k-iVbrpxC.i|k}k/icw~kalblcldeyCeejhspdwdlel:i;iufvfwfxf=iyfzfAfBftbfegeCfDfEfhekhFfGftpncUsflglhlilupvpwpHfIf?izCxpyplhmhnhohzpApBpCpDp@iocphqhiejerhjlJfKfLfMfmdNfklOfPfpcndodpdke'c(cWb)c*c+cEpqcVsllmlnlolACFpGpHpIpQfRf[iWsBCJpKp, rcsc,cqdrdsdtdbbudvdleSfTfmeUfVfpltc]i^iWfXf_iLpshthuhMpYfnevhNpwhxhOpucqlrlsltlPpQpRpZf0f`iSpTp{iyhubulewzhXsAhBhChYs|i}i~iajwdfwxd1fvlZsbjcjUpVpwlvc0sIRJRxlCCylzlAlDCWpXpYpZp2f3fdj1sECgw0p1pXb4f5fBlDhEhFhoe6fejGhHh7f= 8fpeydzdqefjresete9fwcClxcAdgjhjuevevbwbYbcbdbebfbijxbIhJhKhLhjj2p3pBdweMh2s4p5p6pDlyc3sElFlGlHlFC7p8p9p!p!fKR#fkjhwGC#p$p%pIlzc4sLRJlHCKlLlMlIC'p(p)p*p$fMR%fljiwJCjw+p,pNlybxeyemj'f(f)fCd*fNh+f,fOlnjZb-pKCojPlQlpjkwRlSlTlUlzeLCAeOh5slwVlWlqjrj-f.f/f:fsj;f=f?f@fzbBeCe[f]f^fDePh_f`f.pAc6sXlYlZl0l/p:p;p{f|ftjMC=p?pQhRhShTh@p[p]p^p_pujBcUhVhEeFeWh1l}f~fagbgDdcg2ldgegCcEdFdGdGe-c.c0b/c:c;c`pDc7s3l4l5l6lNC{p|p}p~pfgggvjmwOCaqbq- EcFc=cHdIdJdKdgbLdMdHehgigIejgkgcqGc7l8lXhYh9l8swjxjyjdqlgmgzj9sAjBjeqHc!l#l$l%lfqgqhqngogCjiqjqDjZhAb'lnw0h!s1h2h3h#sEjFjGjHjNdowOdpgkq$sIjJjlqNRORPdQdJeKepwqwmq(lIc%sPRPC)lQC*l+l,lRCnqoqpqqqqgrgKj's(sQRrwswRRSCtwrqsqtq-lJc)sSRTR.lTC/l:l;lUCuqvqwqxqsgtgLj*sVCuwyqzqAq=lKc+sURWC?lXC@l[l]lYCBqCqDqEqugvgMj,sZCvwFqGqHq^lLc-sVR0C_l1C`l{l|l2CIqJqKqLqwgxgNj.s3CwwMqNqOq}lMc/sWR4C~l5Cambmcm6CPqQqRqSqygzgOj:s7CxwTqUqVqdmNc;sXR8Cem9Cfmgmhm!CWqXqYqZqAgBgPj=s#Cyw0q1q2qimOc?sYRZRjm$Ckmlmmm%C3q4q5q6qCgDgQjzwAw'CBw7q8q9qnmPc@s0R1Rom(Cpmqmrm)C!q#q$q%qEgFgRjCwDw*CEw'q(q2R3RFw4R5R6R7R8R9R!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~RaSbSGwHw]jcSdSeSfSgShSiSjSkSlSmSnSoSIwJwKwLwMwNwOwPwpSqSrSsStS[suSvSwSxSySzSASBSCSDSESFSGSHSISJSKSLSMSNSOSPSQSRSSSTSUSVSWSXSQwRwSwTwUwVwWwXwYwZw0w1w2w3w4w5w6w7w8w9w!w#w$w%w'w(w)w*w+w,w-w.w/w:w;w=w?w@wYSZS0S[w]w^w1S2S3S4S5S6S7S8S9S!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~SaTbTcTdTeTfTgThTiTjTkTlTmTnToTpTqTrTsTtTuTvTwTxTyTzTATBTCTDTETFTGTHTITJTKTLTMTNTOTGgHgIgJgKgLgMgNgOgPgQgRgSgTgUgVgWgXgYgZg0g1g2g3g4g5g6gPTQTRTSTTTUTVTWTXTYTZT0T1T2T3T4T5T6T7T8T9T!T
34cdef CUresult cuDeviceGetName(char* name, int len, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
35 return _driver._cuDeviceGetName(name, len, dev) 2WnJQ%5)q`cbs_w`w{w+e,eH BbSj*q+q,qTj-q.q/q7n.gKs|w}w~wMiaxbcUjJbKbobccdcec-eNi.eOimu#T;uPC
38cdef CUresult cuDeviceGetUuid(CUuuid* uuid, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
39 return _driver._cuDeviceGetUuid_v2(uuid, dev) 2Wn,r.r0nuk1nvk2nwk3nxk4nyk5nzk6nAkSuTuUuVuWuXuYuZu0u1u2u8nBk9nCk!n#n$n%n'n(n)n*n+n,n-n.nDkEkFkGkHkIkJkKkLkMkNkOk/nPk:nni;nQk=nRk?nSk3u4u@nTk[nUk]nVk5u6u7u8u9u!uNQ'5(5)5*5+C,C=e9c@e[e]e^e!c`e#c{e|e}e~e$caf^g%c4i5i]v^v_v`vpC=k'iUbppvC(i~v)i*i+iaw?k@k[k]k~dwCaehhqpbwTs^k_kPdQdJeKeWC0C4C8C
42cdef CUresult cuDeviceGetLuid(char* luid, unsigned int* deviceNodeMask, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
43 return _driver._cuDeviceGetLuid(luid, deviceNodeMask, dev)
46cdef CUresult cuDeviceTotalMem(size_t* bytes, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
47 return _driver._cuDeviceTotalMem_v2(bytes, dev)
50cdef CUresult cuDeviceGetTexture1DLinearMaxWidth(size_t* maxWidthInElements, CUarray_format format, unsigned numChannels, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
51 return _driver._cuDeviceGetTexture1DLinearMaxWidth(maxWidthInElements, format, numChannels, dev)
54cdef CUresult cuDeviceGetAttribute(int* pi, CUdevice_attribute attrib, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
55 return _driver._cuDeviceGetAttribute(pi, attrib, dev) 2a Ou2 QcCbc C RdDb1bI 2b5 ?c? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S -C.C]skubx/Ccx%m^j'm_j(m)m^sSdTdUdLe' +5,54b5b6bSc7b@ [ ] ibTcUcVc@c-5_s`s{s|s}s~sVjsm*m+m`b`jZe0e{j)d1eoipiqiri=m?m{b|j2e3e}j*d4esitiuivi{m~j|mak}m~manbkbnckcndnenfn|bdk5e6eek+d7ewixiyizimnnn}bfk8e9egk,d!eAiBiCiDiunvn~bhk#e$eik-d%eEiFiGiHiCnDnacjk'e(ekk.d)eIiJiKiLiKnlkLnmkMnNnOnnkPnokQnRnSnpkTnqkUnVn.5tmatMe/5Vd:5$T%T'T(T)T*T8b9b!b#b$b%b/ NeOe3 T L bt7g6 jbEb'b8g9gU V W !gX Y 7 8 #g$g9 (b4 M D J K b B ZB0B1B2B3B4By 5B^ 6Bz 7BA 8BE 9Bkb!BF #BG $BZ %B0 'B1 (B)B*B+B,B-B.B/BN ( ) )bWcXcYc! PeQeWjXjYj%gZj0j(r)r*r+r-r/r:r;rctXnrkQuYnskZntkRu=r?r@r[r]r^r_r`r{r0nuk1nvk2nwk3nxk4nyk5nzkH 6nBbAkSuTuUuVuWuXuYuZu0u1u2u8nBk9nCk!n#n$n%n'n(n)n*n+n,n-n.nDkEkFkGkHkIkJkKkLkMkNkOk/nPk:nni;nQk=nRk?nSk3u4u@nTk[nUk]nVk5u6u7u8u9u!umu:q:C;C4h5h=C?C@C[C]C^C_C`C{C#u|C}C~CaDbDcDdDeDfDgDhDiDjDkD$ulDmDnDoDpDqDrDsDtDuDvDwDxDyDzDADBDCDDDEDFDGDHDIDJDKDLDMDNDODPDQDRDSD%uTDUDVDWD'uXDYDZD0D1D2D3D(u4D5D)u6D7D8D9D*u!D+u#D$D%D'D(D)D*D+D,D-D.D/D,u:D;D-u=D?D@D[D]D^D_D`D{D.u|D}D~DaEbEcEdEeEfEgEhEiE/ujEkE:ulEmEnEoEpEqErEsEtEuEvEwExEyEzEAEBE+ Fb[c*b/e# _n$ `n;5=5+bReSe1j2j3j4j'g5j6jTe}c~cadbdcd=u?u@u[u]u^u_u`u{u|u}u~uavbvcvdvevfvgvhvivjvkvlvmvnvovpvqvrvsvtvuvvvwvxv6h7j;e8jjCfc+T,TumdddxvmexPiQiRifxRb9j/dwmSi=e9cTi@eUi[eVi]e^e!cWi:g;gCEedDE=gEE?gFE@gGE[gHEfdIE]gJEXi`e:d#cYi{eZi|e0i}e1i~e;d$c2iaf^g_g3igd=d-T7h!jxmgc%c?d|n4i5i.TWd8c/ThcKE:T}n~ndtaoetbocodo: eomiftgthtitjtktltmtntotfogohoio-v.v/v:v;v=v?v@v[vlbmbLEjoMEkoNEloOEmoPEnoQEoogxpohxqoixrojxsokxtolxuomxvonxwooxxopxyoqxzorxAosxBotxCouxDovxEowxFoxxGoHoIoREJoSEKoTELoUEMoVENoWEOoXEPoYEQoZERo0ESo1ETo2EUo3EVo4EWo5EXo6EYo7EZo8E0o9E1o!E2o#E3o4o5o6o7o8o9o!o#o$o%o'o(o)o*o+o,o-o.o]v^v_vlC`v?o7kic8k#k^ocfdf6iNs$k{o|o%kjc'k*kbpefff7iPsSbgfhf+k{g|g}g@dif8i~gahjf; kf[dhdid]d9i^d_d`dlfkc,klcjdbh!i{d|dpbqbTb| } ~ ab#irbchfhkd}dghip-kmc.k;kmpmfnf%iSs=k'iUb(i+i]k~daehhqp`ksbbece,iofpfqfldrfihsftf{k-iVb.i/icldeeejhsptbfegeCfDfEfhekhFfGftpncflilHfIf?i@iocphqhiejerhjlJfKfLfMfmdNfklOfPfpcndodpdke'c(cWb)c*c+cEpqcllolIpQfRf[iWs, rcsc,cqdrdsdtdbbudvdleSfTfmeUfVfpltc]i^iWfXf_iLpshthuhMpYfnevhNpwhxhOpucqltlZf0f`i{iyhubzhChajwdxd1fvlVpwlvcxlAlZp2f3fdj1sXb4f5fBlDhEhFhoe6fejGhHh7f= 8fpeydzdqefjresete9fwcClxcAdgjhjuevevbwbYbcbdbebfbijxbIhLhBdweMh6pDlycElHl!p!f#fkjhw%pIlzcJlMl*p$f%fljiwNlybxeyemj'f(f)fCd*fNh+f,fOlnjZbojpjUlzeAeOh5szbBeCe[f]f^fDePh_f`f.pAcXl0l{f|ftjujBcUhVhEeFeWh1l}f~fagbgDdcg2ldgegCcEdFdGdGe-c.c0b/c:c;c`pDc3l6l~pfgggvjmw- EcFc=cHdIdJdKdgbLdMdHehgigIejgkgcqGc7l8lXhYh9l8swjxjyjdqlgmgzj9sAjBjeqHc!l%lngogCjDjZhAb0h3hHjNdOdpgkqPdQdJeKepwqwmq(lIc)l,lqqqgrgKj's(srwswtq-lJc.l;lxqsgtgLj*sAq=lKc?l]lEqugvgMj,sHq^lLc_l|lLqwgxgNj.sOq}lMc~lcmSqygzgOj:sVqdmNcemhmZqAgBgPj=s2qimOcjmmm6qCgDgQjzwAw9qnmPcomrm%qEgFgRjCwDw;T=TFw?T@T[TGwHw]jIwJwKwLwMwNwOwPw]T[syxySQwRwSwTwUwVwWwXwYwZw0w1w2w3w4w5w6w7w8w9w!w#w$w%w'w(w)w*w+w,w-w.w/w:w;w=w?w@w[w]w^w% XdymzmAmBmCmDmEmFmGmHmImJm8h9hGgHgIgJgKgLgMgNgOgPgQgRgSgTgUgVgWgXgYgZg0g1g2g3g4g5g6g;q=q,b
58cdef CUresult cuDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, CUdevice dev, int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
59 return _driver._cuDeviceGetNvSciSyncAttributes(nvSciSyncAttrList, dev, flags)
62cdef CUresult cuDeviceSetMemPool(CUdevice dev, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
63 return _driver._cuDeviceSetMemPool(dev, pool) 2^T
66cdef CUresult cuDeviceGetMemPool(CUmemoryPool* pool, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
67 return _driver._cuDeviceGetMemPool(pool, dev) 28b/ 3 T L 'b8g9gU V W !gX Y 7 8 #g$g9 Zc0c1cy ^ z A E kbF G 4h5h*b# $ 6h7j;e8jiC$E9j7h: lbmb7k$k%kjf; kf[dhdid]d9i^d_d`dlfkc,klcjdbh!i{d|d-k'i-iyhwl7f= 8fpeydzdqefjresete9fwcClxcAdgjhjueveDlIlnjZh(l-l=l^l}ldmimnm% XdymzmAmBmCmDmEmFmGmHmImJm8h9hGgHgIgJgKgLgMgNgOgPgQgRgSgTgUgVgWgXgYgZg0g1g2g3g4g5g6g;q=q,b
70cdef CUresult cuDeviceGetDefaultMemPool(CUmemoryPool* pool_out, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
71 return _driver._cuDeviceGetDefaultMemPool(pool_out, dev) 2^T
74cdef CUresult cuDeviceGetExecAffinitySupport(int* pi, CUexecAffinityType type, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
75 return _driver._cuDeviceGetExecAffinitySupport(pi, type, dev)
78cdef CUresult cuFlushGPUDirectRDMAWrites(CUflushGPUDirectRDMAWritesTarget target, CUflushGPUDirectRDMAWritesScope scope) except ?CUDA_ERROR_NOT_FOUND nogil:
79 return _driver._cuFlushGPUDirectRDMAWrites(target, scope)
82cdef CUresult cuDeviceGetProperties(CUdevprop* prop, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
83 return _driver._cuDeviceGetProperties(prop, dev)
86cdef CUresult cuDeviceComputeCapability(int* major, int* minor, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
87 return _driver._cuDeviceComputeCapability(major, minor, dev)
90cdef CUresult cuDevicePrimaryCtxRetain(CUcontext* pctx, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
91 return _driver._cuDevicePrimaryCtxRetain(pctx, dev) 2nuoupuqurusutuuuvuwuxuyuzuAuBuCu'rDuEuFuGuHuIuJuKuLuMuNu(g
94cdef CUresult cuDevicePrimaryCtxRelease(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
95 return _driver._cuDevicePrimaryCtxRelease_v2(dev) 2?5@5[5]5^5_5`5{5|5}5~5a6b6c6d6e6'rf6g6h6i6j6k6l6m6n6o6p6q6
98cdef CUresult cuDevicePrimaryCtxSetFlags(CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
99 return _driver._cuDevicePrimaryCtxSetFlags_v2(dev, flags)
102cdef CUresult cuDevicePrimaryCtxGetState(CUdevice dev, unsigned int* flags, int* active) except ?CUDA_ERROR_NOT_FOUND nogil:
103 return _driver._cuDevicePrimaryCtxGetState(dev, flags, active)
106cdef CUresult cuDevicePrimaryCtxReset(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
107 return _driver._cuDevicePrimaryCtxReset_v2(dev)
110cdef CUresult cuCtxCreate_v2(CUcontext* pctx, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
111 return _driver._cuCtxCreate_v2(pctx, flags, dev)
114cdef CUresult cuCtxCreate_v3(CUcontext* pctx, CUexecAffinityParam* paramsArray, int numParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
115 return _driver._cuCtxCreate_v3(pctx, paramsArray, numParams, flags, dev)
118cdef CUresult cuCtxCreate(CUcontext* pctx, CUctxCreateParams* ctxCreateParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
119 return _driver._cuCtxCreate_v4(pctx, ctxCreateParams, flags, dev) 2SATAUAVAWAXAYAZA0A1A2A3A4A5A6A7A8A9A!A#A$A%A'A(A)A*A+A,A-A.A/A:A;A=A?A@A[A]A^A_A`A{A|A}A~AaB
122cdef CUresult cuCtxDestroy(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
123 return _driver._cuCtxDestroy_v2(ctx) 2r6s6t6u6v6w6x6y6z6A6B6C6D6E6F6G6H6I6J6K6L6M6N6O6P6Q6R6S6T6U6V6W6X6Y6Z6061626364656
126cdef CUresult cuCtxPushCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
127 return _driver._cuCtxPushCurrent_v2(ctx) 2%E_T
130cdef CUresult cuCtxPopCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
131 return _driver._cuCtxPopCurrent_v2(pctx) 2`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHUIUJUKULUMUNUOUPUQURUSUTUUUVUWUXUYU'E(E)E*EZU+E,E-E.E/E:E;E=E?E@E[E]E^E_E`E{E|E0U}E~EaFbFcFzxdFeF1UfFgFhFiFjFkFlFmFnFoFpFqFrFsF2UtFuFvFwFxFyFzFAFBFCFDFEFFFGF3UAxBxHFIF4UJFKFLFMFNFOFPFQFRFSFTFUFVF5UCxDxWFXF6UYFZF0F1F2F3F4F5F6F7F8F9F!F#F$F%F'F(F)F*F+F,F-F.F/F:F;FExFx=F?F@F[F]F^F_F`F{F|F}F~FaGbGcGdGeGGxHxfGgGhGiGjGkGlGmGnGoGpGqGrGsGtGuGvGIxJxwGxGyGzGAGBGCGDGEGFGGGHGIGJGKGLGMGKxLxNGOGPGQGRGSGTGUGVGWGXGYGZG0G1G2G3G4G5G6G7G8G9G!G#G7U$G%G'G(G)G*G8U9U!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~VaWbWcWdWeWfWgWhWiWjWkWlWmWnWoWpWqWrWsWtWuWvWwWxWyW+G,G-G.G/GzWAW:G;GBW=G?G@G[GCW]G^GDWEWFWGWHWIWJWKW|r}r~rascsdsesfsgshsisjsLWMWNWOWPWQWRWSWTWUWVWWWXWYWZWkslsmsnsospsqsrssstsusvswsxsyszsAsBsCsDsEsFsGsHsIsJs0W1W2W3W4W5W6W7W8W9W!W#W$W%W'W(W)W*W+W,W-W.W/W:W;W=W?W@W[W]W^W_W`W{W|W}W~WaXbXcXdXeXfXgXhXiXjXkXlXmXnXoXpXqXrXsXtXuXvXwXxXyXzXAXBXCXDXEX_G`G{GFXGX%E|G}G~GHXaH_TbHcHIXJXKXLXMXNXOXPXQXRXSXTXUXVXWXXXYXZX0X1X2X3X4X5X6X7X8X9X!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~Za0b0c0d0e0f0g0h0i0j0k0l0m0n0o0p0q0r0s0t0u0v0w0x0y0z0A0B0C0D0E0dHeHfHgHF0G0hHiHMxNxjHkHlHmHnHH0oHpHqHI0rHsHtHuHvHJ0wHxHyHzHAHK0L0BHCHOxPxDHEHFHGHHHM0IHJHKHN0LHMHNHOHPHQxRxQHRHSHTHUHVHWHXHYHSxTxUxVxptqtWxXxYxZx0xZH1x0H2x3x1H4x5x6x7x8x2H3H4H5H6H7H8H9H9x!x!H#H$H%H'H(H)H*H+H,H-H.H/H:H;H#x$x=H?H@H[H]HO0^HP0_H`HQ0{H|H}H~HaIbIcIR0dIeI%x'xfIgIhIiIjIS0kIT0lImIU0nIoIpIqIrIsI(x)xtIuIvIwIxIyIzIAIBI*x+x,x-xCI.x/x:x;x=x?x@x[xDI]xEI^x_xFI`x{x|x}x~xaybycydyeyfygyhyiyGIjykyHIIIJIKILIMINIOIPIQIRIlymySITIUIVIWIXIYIZI0I1I2I3I4I5I6I7I8I9I!I#I$I%I'Inyoy(I)I*I+I,I-I.I/I:I;I=I?Ipyqy@I[I]I^I_I`I{I|I}I~IaJbJrysycJdJeJfJgJV0hJiJjJW0kJlJmJnJtyuyoJpJqJrJsJtJvywyuJvJwJxJyJzJAJBJCJDJxyyyEJFJGJHJIJX0JJKJLJMJNJOJPJQJRJzyAySJTJUJVJWJXJYJZJ0JByCyDyEy1JFyGyrtstHyIyJyKyLy2JMy3JNyOy4JPyQyRy5J6J7J8J9JY0Z0!J#JSyTy$J%J'J(J)J00*J+J,J10-J.J/J:J;JUyVy=J?J@J[J]J^J_J`J{JWyXyYyZyttut0y1y2y3y4y|J5y}J6y7y~J8y9y!y#y$yaKbKcKdKeKfKgKhK%y'yiKjKkKlKmKnKoKpKqKrKsKtKuKvKwK(y)yxKyKzKAKBK20CK30DKEK40FKGKHKIKJKKKLK50MKNK*y+yOKPKQKRKSK60TK70UKVK80WKXKYKZK0K1K,y-y2K3K4K5K6K7K8K9K!K.y/y:y;y#K=y?y@y[y]y^y_y`y$K{y%K|y}y'K~yazbzczdzezfzgzhzizjzkzlzmz(Knzoz)K*K+K,K-K.K/K:K;K=K?Kpzqz@K[K]K^K_K`K{K|K}K~KaLbLcLdLeLfLgLhLiLjLkLlLmLrzsznLoLpLqLrLsLtLuLvLwLxLyLtzuzzLALBLCLDLELFLGLHLILJLKLvzwzLLMLNLOLPL90QLRLSL!0TLULVLWLxzyzXLYLZL0L1L2LzzAz3L4L5L6L7L8L9L!L#L$LBzCz%L'L(L)L*L#0+L,L-L.L/L:L;L=L?LDzEz@L[L]L^L_L`L{L|L}LFzGzHzIz~LJzKzvtwtLzMzNzOzPzaMQzbMRzSzcMTzUzVzdM$0%0'0(0)0*0+0,0eMfMgMhM-0.0iMjMWzXzkMlMmMnMoM/0pMqMrM:0;0=0?0@0[0sMtMuMvMwMxMyMzM]0^0AMBMYzZzCMDMEMFMGM_0HMIMJM`0KMLMMMNMOMPMQMRM{0|0SMTM0z1zUMVMWMXMYM}0ZM0M1M~02M3M4M5M6M7M8M9Ma1b1!M#M2z3z$M%M'M(M)Mc1*M+M,Md1-M.M/M:M;M=M?M@Me1f1[M]M4z5z^M_M`M{M|Mg1}M~MaNh1bNcNdNeNfNgNhNiNi1j1jNkN6z7zlNmNnNoNpNk1qNrNsNl1tNuNvNwNxNyNzNANm1n1BNCN8z9zDNENFNGNHNo1INJNKNp1q1LNMNNNONPNQNRNSNr1s1TNUN!z#zVNWNXNYNZNt10N1N2Nu1v13N4N5N6Nw1x1y1z1A1B1C1D1E1F1G1H1I1J1K1L1M1N1O1P1Q1R1S1T1U1V1W1X1Y1Z101112131415161718191!1#1$1%1'1(1)1*1+1,1-1.1/1:1;1=1?1@1[1]1^1_1`1{1|1}1~1a2b2c2d2e2f2g2h2i2j2k2l2m2n2o2p2q2r2s2t2u2v2w2x2y2z2A2B2C2D2E2F2G2H2I2J2K2L2M2N2O2P2Q2R2S2T2U2V2W2X2Y2Z202122232425262728292!2#2$2%2'2(2)2*2+2,2-2.2/2:2;2=2?2@2[2]2^2_2`2{2|2}2~2a3b3c3d3e3f3g3h3i3j3k3l3m3n3o3p3q3r3s3t3u3v3w3x3y3z3A3B3C3D3E3F3G3H3I3J3K3L3M3N3O3P3Q3R3S3T3U3V3W3X3Y3Z303132333435363738393!3#3$3%3'3(3)3*3+3,3-3.3/3:3;3=3?3@3[3]3^3_3`3{3|3}3~3a4b4c4d4e4f4g4h4i4j4k4l4m4n4o4p4q4r4s4t4u4v4w4
134cdef CUresult cuCtxSetCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
135 return _driver._cuCtxSetCurrent(ctx) 2NOOOPOQOROSOTOUOVOWOXOYOZO0O1O2O3O4O5O6O7O8O9O!O#O$O%O'O(O)O*O+O,O-O.O/O:O;O=O?O@O[O]O^O_O`O{O|O}O~OaPbPcPdPePfPbBcBdBeBgPfBgBhBiBjB%m^j'mkB_j(m)mlBmBnBoBpBhPqBrBsBtBuBvBwBxByBzBx4ABBBCBDBEBFBGBHBIBJBKBLBMBNBOBPBQBRBSBTBUBVBWBXB*m+m`b`jZe0e{j,m-m.m/m)d1eoipiqiri:m;m=m?m{b|j2e3e}j@m[m]m^m*d4esitiuivi_m`m{m~j|mYBak}m~manbkbnckcndnenfn|bdk5e6eekgnhninjn+d7ewixiyiziknlnmnnn}bfk8e9egkonpnqnrn,d!eAiBiCiDisntnunvn~bhk#e$eikwnxnynzn-d%eEiFiGiHiAnBnCnDnacjk'e(ekkEnFnGnHn.d)eIiJiKiLiInJnKnlkLnmkMnNnOnnkPnokQnRniPSnpkTnqkUnVnjPkPlPmPnPoPpPqPrPsPtPuPvPwPxPyPzPAPBPCPDPEPFPGPHPIPJPKPLPMPNPOPPPQPRPSPTPUPVPWPXPYPZP0P1P2P3P4P5P6P7P8P9P!P#P$P%P'P(P)P*P+P,P-P.P/P:P;P=P?P@P[P]P^P_P`P{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQqQrQsQ66tQuQvQZB0B1B2B3B4B5B6B7B8B9B!B#B$B%B'B(B)B*B+B,B-B.BwQ/BxQyQzQAQBQCQDQEQ7686FQGQ(r)rHQ*r+r-r/r:r;rctIQXnrkQuYnskZntkRu=r?r@r[r]r^r_r`r{r#j960nuk1nvk2nwk3nxk4nyk5nzk6nAkSuTuUuVuWuXuYuZu0u1u2u7n8n.gBk9nCk!n#n$n%n'n(n)n*n+n,n-n.nDkEkFkGkHkIkJkKkLkMkNkOk/nPk:nni;nQk=nRkKQLQMQJb?nKbSk3u4u@nTk[nUk]nVk5u6u7u8u9u!uOQPQQQRQSQTQUQnuoupuqurusutuuuvuwuxuyuzuAuBuCu'rDuEuFuGuHuIuJuKuLuMuNu4h5h!6#6VQ$6%6'6(6WQ)6*6#T7N+6,6{c+ |c-6^nXQ.6YQZQ0Q1Q2Q3Q4Q5Q/6:66Q7Q8Q9Q!h?q#h$h@q(g%h'h$j(h)h*hKm:BWkXk/e_n`nYkZk0k!Q1k2k3k;B=B?B@B[B]B^B_B`B{B|B}B~BaCbCcCdCeCfCgChC#Q+b%j:eTe;6=6?6@6+h,h}c-h~c.h/had:h;h=h?h@h[h]h^h_hbd`h{h|h}h~haibicidieicdfi=u?u@u[u]u^u_u`u{u|u}u~uavbvcvdvevfvgvhvivjvkvlvmvnvovpvqvrvsvtvuvvvwvxvLmUeVe$zy4xt4k%z6h7jLs'z(z)z*z+zyvzvz4AvA4BvB4CvC4DvD4E4EvFvF4G4GvHvIvH4JvI4J4K4KvLvL4MvNvOvM4PvN4QvRvO4SvP4TvQ4UvR4VvS4T4U4WvXvV4W4X4YvY4Z4041424Zv0v3444541v2v64743v4v5v6v8494!4#4$4%47v'48v9v(4!v)4*4#v$v%v+4,4-4'v(v.4)v*v/4:4+v;4/g;e8jjCfc[6$Q+T,T%Q]6umdddx^6vm_6ex`6Pi'QQi(QRi{6fx)QRb|69j}6/d~6wm*QSi+Q=e,Q?ea79cb7Tic7@ed7Uie7[ef7Vig7]eh75ki7^ej7_ek7!cl7Wim7:gn7;g-Qo7ed.Qp7=gq7r7?g/Qs7@g:Qt7[gu7;Qfd=Qv7]gw7x7Xiy7`ez7:dA7#c?QYi@Q{eB7Zi[Q|eC70iD7}eE71i]Q~eF7;dG7$cH72iI7afJ7^g^Q_g_Q3iK7bfL7gd`Q=d{Q-T8N{n`g[q7h!jxm|QgcM7%c?d}QN7O7~QP7Q7WeWd8caRhcKEbRcRdReRfRgRhRiRjRkRlRmRnRoR}n~npRaoqRbocodorReosRtRuRvRwRxRyRR7zRARBRfogohoio-v.v/v:v;v=v?v@v[vCRDRjokolomonooopoqorosotouovowoxoyozoAoBoCoDoEoFoGoHoIoJoKoLoMoNoOoPoQoRoSoToUoVoWoXoYoZo0o1o2o3o4o5o6o7o8o9o!o#o$o%o'o(o)o*o+o,o-o.o/o]v:o^v;o_v'jlC=o`v?o7kicMsERFR8kmC9k!k#knC@o[o]o^ocfdf6iNsoC{v_o`o$k{o|v|o%kjcOsGRpC'kqC(k)k*krC}o~oapbpefff7iPssC}vcpdpSbgfhf+k{g|g}g@dif8i~gahjf; kf[dhdid]d9i^d_d`dlfkc,klcjdbh!i{d|dpbqbTb| } ~ ab#irbchdhehfh$iepfpkd}dghQsgphpip-kmcRs.k/k:k;ktCjpkplpmpmfHRnf%iSsuCnpop=k'iUbppvC(i~v)i*i+iaw?k@k[k]k~dwCaehhqpbwTs^k_k`ksbbece,iofpfqfldrfihsftf{k-iVbrpxC.i|k}k/icw~kalblcldeyCeejhspdwdlel:i;iufvfwfxf=iyfzfAfBftbfegeCfDfEfhekhFfGftpncUsflglhlilupvpwpHfIf?izCxpyplhmhnhohzpApBpCpDp@iocphqhiejerhjlJfKfLfMfmdNfklOfPfpcndodpdke'c(cWb)c*c+cEpqcVsllmlnlolACFpGpHpIpQfRf[iWsBCJpKp, rcsc,cqdrdsdtdbbudvdleSfTfmeUfVfpltc]i^iWfXf_iLpshthuhMpYfnevhNpwhxhOpucqlrlsltlPpQpRpZf0f`iSpTp{iyhubulewzhXsAhBhChYs|i}i~iajwdfwxd1fvlZsbjcjUpVpwlvc0sIRJRxlCCylzlAlDCWpXpYpZp2f3fdj1sECgw0p1pXb4f5fBlDhEhFhoe6fejGhHh7f= 8fpeydzdqefjresete9fwcClxcAdgjhjuevevbwbYbcbdbebfbijxbIhJhKhLhjj2p3pBdweMh2s4p5p6pDlyc3sElFlGlHlFC7p8p9p!p!fKR#fkjhwGC#p$p%pIlzc4sLRJlHCKlLlMlIC'p(p)p*p$fMR%fljiwJCjw+p,pNlybxeyemj'f(f)fCd*fNh+f,fOlnjZb-pKCojPlQlpjkwRlSlTlUlzeLCAeOh5slwVlWlqjrj-f.f/f:fsj;f=f?f@fzbBeCe[f]f^fDePh_f`f.pAc6sXlYlZl0l/p:p;p{f|ftjMC=p?pQhRhShTh@p[p]p^p_pujBcUhVhEeFeWh1l}f~fagbgDdcg2ldgegCcEdFdGdGe-c.c0b/c:c;c`pDc7s3l4l5l6lNC{p|p}p~pfgggvjmwOCaqbq- EcFc=cHdIdJdKdgbLdMdHehgigIejgkgcqGc7l8lXhYh9l8swjxjyjdqlgmgzj9sAjBjeqHc!l#l$l%lfqgqhqngogCjiqjqDjZhAb'lnw0h!s1h2h3h#sEjFjGjHjNdowOdpgkq$sIjJjlqNRORPdQdJeKepwqwmq(lIc%sPRPC)lQC*l+l,lRCnqoqpqqqqgrgKj's(sQRrwswRRSCtwrqsqtq-lJc)sSRTR.lTC/l:l;lUCuqvqwqxqsgtgLj*sVCuwyqzqAq=lKc+sURWC?lXC@l[l]lYCBqCqDqEqugvgMj,sZCvwFqGqHq^lLc-sVR0C_l1C`l{l|l2CIqJqKqLqwgxgNj.s3CwwMqNqOq}lMc/sWR4C~l5Cambmcm6CPqQqRqSqygzgOj:s7CxwTqUqVqdmNc;sXR8Cem9Cfmgmhm!CWqXqYqZqAgBgPj=s#Cyw0q1q2qimOc?sYRZRjm$Ckmlmmm%C3q4q5q6qCgDgQjzwAw'CBw7q8q9qnmPc@s0R1Rom(Cpmqmrm)C!q#q$q%qEgFgRjCwDw*CEw'q(q2R3RS74R5RT7U76R7RV78R9R!RW7#R$R%R'R(R)R*R+R,RX7-R.R/R:R;R=R?R@R[R]R^R_R`R{R|R}R~RaSbScSdSY7eSfSgShSiSjSkSlSmSnSoSZ7pS07qSrSsS1727tS[s37uSvSwSxS=4zSASBSCSDSESFSGSHSISJSKSLSMSNSOSPSQSRSSSytTSUSVSWSXSQwRwSwTwUwVwWwXwYwZw0w1w2w3w4w5w6w7w8w9w!w#w$w%w'w(w)w*w+w,w-w.w/w:w;w=w?w@wYSZS0S[w]w^w1S2S3S4S5S6S7S8S9S!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~SaTbTcTdTeTfTgThT47iTjTkTlTmTnToTpTqTrTsTtTuTvTwTxTyTzT5767AT77BTCTDTET8797FT!7GTHTITJTKT#7$7LT%7'7(7MTNTOTGgztHgAtIgJgKgLgBtMgNgCtOgDtPgQgRgSgTgUgEtFtVgGtWgXgHtYgItZg0g1g2g3g4gJt5g6gKt)7*7+7PT,7QTRTSTTTUT-7.7/7VTWTXT:7;7YTZT0T=71T?7@72T3T4T5T[7]7^76T7T8T9T_7!T
138cdef CUresult cuCtxGetCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
139 return _driver._cuCtxGetCurrent(pctx) 2a Ou`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHUIUJUKULUMUNUOUPUQURUSUTUUUVUWUXUYU'E(E)E*EZU+E,z,E-E.E/E:E;E=E?E@E[E]E^E_E`E{E|E0U}E~EaFbFcFzxdFeF1UfFgFhFiFjFkF@ lF[ mF] nFiboFTcpFUcqFVcrF@csF2UtFuFvFwFxFyFzFAFBFCFDFEFFFGF3UAxBxHFIF4U.mJF/mKFLF1eMFoiNFpiOFqiPFriQF:mRF;mSFTFUFVF5UCxDxWFXF6U]mYF^mZF0F4e1Fsi2Fti3Fui4Fvi5F_m6F`m7F8F9F!F#F$F%F'F(F)F*F+F,F-F.F/F:F;FExFx=F?F@Fin[Fjn]F^F7e_Fwi`Fxi{Fyi|Fzi}Fkn~FlnaGbGcGdGeGGxHxfGgGhGqniGrnjGkG!elGAimGBinGCioGDipGsnqGtnrGsGtGuGvGIxJxwGxGyGynzGznAGBG%eCGEiDGFiEGGiFGHiGGAnHGBnIGJGKGLGMGKxLxNGOGPGGnQGHnRGSG)eTGIiUGJiVGKiWGLiXGInYGJnZG0G1G2G3G4G5G6G7G8G9G!G#G7U$G%G'G(G)G*G9m8U9U!U#U$U-z%U'U(U)U*U+U,U-U.U!m/U:U;U=U?U@U[U]U^U8b_U`U]q{U^q|U_q}U`q~U9baV!bbV#bcV$bdVeVfVgVhViVjV/ kVlVmVnVYdoVZdpV0dqV1drV2dsV3dtV4duV5dvVwVxVyVzVAVBVCV3 DVEVFVGVHVIVJVKV'bLVMVNVU OVV PVW QVRVX SVY TV7 UV8 VVWVXV9 YVZV0V1V2V3V4V(j5V6V7V8V9V!V#V$V%V'V(V)Vb *V+V7c,V-V.V/V:V;V=V?V@V[V]V^V_V`V{V|V}V~VaWbWcWdWeWfWgWhWiWjWkWlWmWnWoWpWqWrWsWtWuWvWwWxWyW+G,G-G.G/GzWAW:G;GBW=G?G@G[GCW]G^GDWEWFWGWHWIWJWKW|r}r~rascsdsesfsgshsisjsLWMWNWOWPWQWRWSWTWUWVWWWXWYWZWkslsmsnsospsqsrssstsusvswsxsyszsAsBsCsDsEsFsGsHsIsJs0W1W2W3W4W5W6W7W8W9W!W#W$W%W'W(W)W*W+W,W-W.W/W:W;W=W?W@W[W]W^W_W`W{W:C;C4h|W5h}W~WaXbXcXdXeXfXgXhXiX?4=C?C@C[C]C^C_C`C{C@4#u|C}C~CaDbDcDdDeDfDgDhDiDjDkD$ulDmDnDoDpDqDrDsDtDuDvDwDxDyDzDADBDCDDDEDFDGDHDIDJDKDLDMDNDODPDQDRDSD%uTDUDVDWD'uXDYDZD0D1D2D3D(u4D5D)u6D7D8D9D*u!D+u#D$D%D'D(D)D*D+D,D-D.D/D,u:D;D-u=D?D@D[D]D^D_D`D{D.u|D}D~DaEbEcEdEeEfEgEhEiE/ujEkE:ulEmEnEoEpEqErEsEtEuEvEwExEyEzEAEBEjX7NkXlXmX;u[4+C`7,C{c+ |cnX^noXpXqXrXsXtXuXvXwXxXyXzXAXBXCXDXMmEX_G`G{G# FX$ GX%E|G}G~GHXaHbHcHIXJXKXLXMXNXOXPXQXRXSXTXUXVXWXXXYXZX0X1X2X3X:e4X5X6X7X}c~cadbdcd8X9X!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~XaYbYcYdYeYfYgY4kyvzvAvBvCvDvEvFvGvHvIvJvKvLvMvNvOvPvQvRvSvTvUvVvWvXvYvZv0v1v2v3v4v5v6v7v8v9v!v#v$v%v'v(v)v*v+v/g;ehYiYjYkYlYmYnYoYpYqYrYsYtYuYvYwYxYyYkCzYAYBYCYDYEYFYGYHYIYJYKYLYMYNYOYPYQYRYSYTYUYVYWYXYYYZY0Y1Y2Y3Y4Y5Y6Y7Y8Y9Y!Y#Y$Y%Y'Y(Y)Y*Y+Y,Y-Y.Y/Y:Y;Y=Y?Y@Y{n[Y]Y?d^Y_Y`Y{Y|Y}Y~YhcaZbZcZdZeZfZgZhZiZjZkZlZmZnZoZpZqZrZsZtZuZvZwZxZmiyZzZAZBZCZDZEZFZGZHZIZJZKZLZMZNZOZPZQZRZSZTZUZVZWZXZYZZZ0Z1Z2Z3Z4Z5Z6Z7Z8Z9Z!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~Za0b0c0d0e0f0g0h0i0j0k0l0m0n0o0p0q0r0s0t0u0v0w0x0y0z0A0B0C0D0E0dHeHfHMsgHF0G0hHiHMxNxjHkHlH[omH]onHH0oHdfpH6iqHI0rHsH_otH`ouHvHJ0wHxHyHzHOsAHK0L0BHCHOxPxDHEHFH~oGHapHHM0IHffJH7iKHN0LHMHcpNHdpOHPHQxRxQHRH|gSH}gTHUHifVH8iWH~gXHahYHSxTxkfUxVxptqtWxXxYx_dZx`d0xZH1x0Hlc2xjd3x1H4x{d5x|d6x7x8x2H| 3H} 4H~ 5Hab6H#i7Hrb8Hch9Hdh9xeh!xfh!H$i#Hep$Hfp%Hkd'H}d(Hgh)HQs*Hgp+Hhp,H-H.H/HRs:H;H#x$x=H?H@Hkp[Hlp]HO0^HP0nf_H%i`HQ0{Hnp|Hop}H~HaIbIppcIR0dIeI%x'xfIgIhI@kiI[kjIS0kIT0aelIhhmIU0nIoI^kpI_kqIrIsI(x)xtIuIpfvIqfwIxIrfyIihzIsfAItfBI*x+x,xrp-xCI.x/x:x;x=x?xal@xbl[xDI]xEIee^xjh_xFI`xdl{xel|x}x~xufayvfbywfcyxfdyeyyffyzfgyAfhyBfiyGIjykyHIDfIIEfJIheKIkhLIFfMIGfNIOIPIUsQIRIlymySITIvpUIwpVIWIIfXI?iYIZIxp0Iyp1Ilh2Imh3Inh4Ioh5Izp6IAp7IBp8ICp9IDp!I#I$Iph%I'Inyoy(I)I*IKf+ILf,I-Imd.INf/I:IOf;IPf=I?Ipyqy@I[I'c]I(c^IWb_I)c`I*c{I+c|I}I~IVsaJbJrysycJdJeJGpfJHpgJV0hJRfiJ[ijJW0kJJplJKpmJ, nJrctyscuy,coJqdpJrdqJsdrJtdsJbbtJudvyvdwyleuJSfvJTfwJmexJUfyJVfzJAJBJ]iCJDJxyyyEJFJGJthHJuhIJX0JJneKJvhLJMJwhNJxhOJPJQJRJzyAySJTJQpUJRpVJWJ0fXJ`iYJSpZJTp0JByCyDyulEy1JFyGyrtstHyIyJy}iKy~iLy2JMy3JxdNy1fOy4JPybjQycjRyUp5J6J7J8J0s9JY0Z0!J#JSyTy$J%J'JXp(JYp)J00*J3f+Jdj,J10-J.J0p/J1p:J;JUyVy=J?JEh@JFh[J]J6f^Jej_JGh`JHh{JWyXy8fYyZyttut0y1y2yse3yte4y|J5y}Jxc6yAd7y~J8yue9yve!y#y$yaKcbbKdbcKebdKfbeKijfKxbgKIhhKJh%yKh'yLhiKjjjK2pkK3plKBdmKwenKMhoK2spK4pqK5prKsKtKuK3svKwK(y)yxKyKzK8pAK9pBK20CK30#fDKkjEK40FK#pGK$pHKIKJKKK4sLK50MKNK*y+yOKPKQK(pRK)pSK60TK70%fUKljVK80WKXK+pYK,pZK0K1K,y-y2K3K(f4K)f5K6K*f7KNh8K+f9K,f!K.y/y:y-p;y#K=y?y@y[y]y^ySl_yTl`y$K{y%KAe|yOh}y'K~yVlazWlbzczdz-fez.ffz/fgz:fhziz;fjz=fkz?flz@fmz(Knzoz)K]f*K^f+KDe,KPh-K_f.K`f/K:K;K6s=K?Kpzqz@K[K:p]K;p^K_K|f`Ktj{K|K=p}K?p~KQhaLRhbLShcLThdL@peL[pfL]pgL^phL_piLjLkLUhlLmLrzsznLoLpL~fqLagrLsLDdtLcguLvLdgwLegxLyLtzuzzLAL-cBL.cCL0bDL/cEL:cFL;cGLHLIL7sJLKLvzwzLLMLNL|pOL}pPL90QLggRLvjSL!0TLaqULbqVL- WLEcxzFcyz=cXLHdYLIdZLJd0LKd1Lgb2LLdzzMdAzHe3Lhg4Lig5LIe6Ljg7Lkg8L9L!L7l#L$LBzCz%L'L(Lxj)Lyj*L#0+Lmg,Lzj-L.LAj/LBj:L;L=L?LDzEz@L[Lgq]Lhq^L_Log`LCj{Liq|Ljq}LFzGzHz'lIz~LJzKzvtwtLzMzNzFjOzGjPzaMQzbMOdRzpgSzcMTzIjUzJjVzlqdM$0%0'0(0)0*0+0,0eMfMgM%shM-0.0iMjMWzXzkMlMmMoqnMpqoM/0pMrgqMKjrM:0;0=0?0@0[0sMtMrquMsqvMwMxMyM)szM]0^0AMBMYzZzCMDMEMvqFMwqGM_0HMtgIMLjJM`0KMLMyqMMzqNMOMPMQM+sRM{0|0SMTM0z1zUMVMWMCqXMDqYM}0ZMvg0MMj1M~02M3MFq4MGq5M6M7M8M-s9Ma1b1!M#M2z3z$M%M'MJq(MKq)Mc1*Mxg+MNj,Md1-M.MMq/MNq:M;M=M?M/s@Me1f1[M]M4z5z^M_M`MQq{MRq|Mg1}Mzg~MOjaNh1bNcNTqdNUqeNfNgNhN;siNi1j1jNkN6z7zlNmNnNXqoNYqpNk1qNBgrNPjsNl1tNuN0qvN1qwNxNyNzN?sANm1n1BNCN8z9zDNENFN4qGN5qHNo1INDgJNQjKNp1q1LNMN7qNN8qONPNQNRN@sSNr1s1TNUN!z#zVNWNXN#qYN$qZNt10NFg1NRj2Nu1v13N4N'q5N(q6Nw1x1Fwy1z1A1B1C1D1E1F1G1H1I1J1K1L1M1N1O1P1Q1R1S1T1U1V1W1X1Y1Z101112131415161718191!1#1$1Gw]4Hw]j%1'1(1)1*1+1,1-1.1/1:1;1=1?1^4Iw_4JwKw`4@1LwMwNwOwPw[1]1^1_1`1{1|1}1[s~1a2b2c2d2e2f2g2h2i2j2k2l2m2Ltn2o2p2q2r2s2t2u2v2w2x2y2z2A2B2C2D2E2F2G2H2I2J2K2L2M2N2O2P2Q2R2S2T2U2V2W2X2Y2Z202122232425262728292!2#2$2%2'2(2)2*2+2,2-2.2/2:2;2=2?2@2[2]2^2_2`2{2|2}2~2a3b3c3d3e3f3g3h3i3j3k3l3m3n3o3p3q3r3s3t3u3v3w3x3y3z3A3B3C3D3E3F3G3H3I3J3K3L3M3N3O3P3Q3R3S3T3U3V3W3X3Y3Z303132333435363738393!3#3$3%3'3(3)3*3+3,3-3.3GgHgIgJgKgLgMgNgOgPgQgRgSgTgUgVgWgXgYgZg0g1g2g3g4g5g6g/3:3;3=3?3@3[3]3^3_3`3{3|3}3~3a4b4c4d4e4f4g4h4i4j4k4l4m4n4o4p4q4r4s4t4u4v4w4
142cdef CUresult cuCtxGetDevice(CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil:
143 return _driver._cuCtxGetDevice(device) 2a Ou-b)j.b/b:b;b)g2 QcCbc 6dC Rd.z*jDb1bI 2b+j5 ?c,j? . /zhb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S -C.C]s{7kubx/Ccx%m^j'm_j(m)m^s7dSdTdUdLe' 2c8d9d4b5b6bSc7b@ [ ] ibTcUcVc@c_s`s{s|s}s~sVjsm*m+m`b`jZe0e{j)d1eoipiqiri=m?m{b|j2e3e}j*d4esitiuivi{m~j|mak}m~manbkbnckcndnenfn|bdk5e6eek+d7ewixiyizimnnn}bfk8e9egk,d!eAiBiCiDiunvn~bhk#e$eik-d%eEiFiGiHiCnDnacjk'e(ekk.d)eIiJiKiLiKnlkLnmkMnNnOnnkPnokQnRnSnpkTnqkUnVntmatMeVd$T%T'T(T)T*T8b]c9b!b#b$b* Gb=b3c4c%b/ giNe-jnbHbOe.j3 T L bt7g6 jbEb'b8g9gU V W !gX Y 7 8 #g$g9 (b?b5c4 M D J K b B y ^ z A E kbF G Z 0 1 |7@b[bN ( ) 6c)bWcXcXeYc! (r)r}7*r+r-r/r:r;rctXnrkQuYnskMtZnNttkRu=r?r@r[r]r^r_r`r{r#jukvkwkxkykzkAkBkCkDkEkFkGkHkIkJkKkLkMkNkOkPkniQkRkSkTkUkVk:z;z=z?z@z[z:C;C4h5h9N]z?4=C?C@C[C]C^C_C`C{C@4#u|C}C~CaDbDcDdDeDfDgDhDiDjDkD$ulDmDnDoDpDqDrDsDtDuDvDwDxDyDzDADBDCDDDEDFDGDHDIDJDKDLDMDNDODPDQDRDSD%uTDUDVDWD'uXDYDZD0D1D2D3D(u4D5D)u6D7D8D9D*u!D+u#D$D%D'D(D)D*D+D,D-D.D/D,u:D;D-u=D?D@D[D]D^D_D`D{D.u|D}D~DaEbEcEdEeEfEgEhEiE/ujEkE:ulEmEnEoEpEqErEsEtEuEvEwExEyEzEAEBE7N;u[4+C,C{c+ |c!N^n#NNmOmPmQmRmSmFbTmUmVmWmXm/jhi[c+b%j:eTe~7a8:j+h,h}c-h~c.h/had:h;h=h?h@h[h]h^h_hbd`h{h|h}h~haibicidieicdfib8=u?u@uc8[u]u^u_u`u{u|u}u~uavbvcvdvevfvgvhvivjvkvlvmvnvovpvqvrvsvtvuvvvwvxvLmUeVe$zy4xt4k%zyvzvz4AvA4BvB4CvC4DvD4E4EvFvF4G4GvHvIvH4JvI4J4K4KvLvL4MvNvOvM4PvN4QvRvO4SvP4TvQ4UvR4VvS4T4U4WvXvV4W4X4YvY4Z4041424Zv0v3444541v2v64743v4v5v6v8494!4#4$4%47v'48v9v(4!v)4*4#v$v%v+4,4-4'v(v.4)v*v/4:4+v;4/g;e8jfcd8umdddxvmexPiQiRifxRb9j/dwmkCSi=e?e9cTi@eUi[eVi]e5k^e_e!cWi:g;gCEedDE=gEE?gFE@gGE[gHEfdIE]gJEXi`e:d#cYi{eZi|e0i}e1i~e;d$c2iaf^g_g3ibfgd=d8N{n`g[q7h!jxmgc%c?d|n4i5i.TYmZmWeWd8c/ThcKE:T}n{4~ndtaoetbo|4co}4do: eomiftgthtitjtktlt^zmtntotfogohoio-v.v/v:v;v=v?v@v[vLEjoMEkoNEloOEmoPEnoQEoogxpohxqoixrojxsokxtolxuomxvonxwooxxopxyoqxzorxAosxBotxCouxDovxEowxFoxxGoe8Hof8IoREJoSEKoTELoUEMoVENoWEOoXEPoYEQoZERo0ESo1ETo2EUo3EVo4EWo5EXo6EYo7EZo8E0o9E1o!E2o#E3og84o~45oa56ob57oc58od59oe5!of5#og5$oh5%oi5'oj5(ok5)ol5*om5+on5,oo5-o.o?oic8k#k^ocfdf6iNs{o|ojc'k*kbpefff7iPsSbgfhf+k{g|g}g@dif8i~gahjf; [d]dlfkclcjdbhpbqbTb| } ~ ab#irbchfhkd}dghipmc.k;kmpmfnf%iSs=kUb(i+i]k~daehhqp`ksbbece,iofpfqfldrfihsftf{kVb.i/icldeeejhsptbfegeCfDfEfhekhFfGftpncflilHfIf?i@iocphqhiejerhjlJfKfLfMfmdNfklOfPfpcndodpdke'c(cWb)c*c+cEpqcllolIpQfRf[iWs, rcsc,cqdrdsdtdbbudvdleSfTfmeUfVfpltc]i^iWfXf_iLpshthuhMpYfnevhNpwhxhOpucqltlZf0f`i{iubzhChajwdxd1fvlVpvcxlAlZp2f3fdj1sXb4f5fBlDhEhFhoe6fejGhHh7f= peqe9fwcxcAdgjvbwbYbcbdbebfbijxbIhLhBdweMh6pycElHl!p!f#fkjhw%pzcJlMl*p$f%fljiwNlybxeyemj'f(f)fCd*fNh+f,fOlZbojpjUlzeAeOh5szbBeCe[f]f^fDePh_f`f.pAcXl0l{f|ftjujBcUhVhEeFeWh1l}f~fagbgDdcg2ldgegCcEdFdGdGe-c.c0b/c:c;c`pDc3l6l~pfgggvjmw- EcFc=cHdIdJdKdgbLdMdHehgigIejgkgcqGc7l8lXhYh9l8swjxjyjdqlgmgzj9sAjBjeqHc!l%lngogCjDjAb0h3hHjNdOdpgkqpwqwmqIc)l,lqqqgrgKj's(srwswtqJc.l;lxqsgtgLj*sAqKc?l]lEqugvgMj,sHqLc_l|lLqwgxgNj.sOqMc~lcmSqygzgOj:sVqNcemhmZqAgBgPj=s2qOcjmmm6qCgDgQjzwAw9qPcomrm%qEgFgRjCwDw;T=TFwh8?T@T[TGw]4Hw]j^4Iw_4JwKw`4i8LwMwNwOwPw]T[syx=4j8_z`z{z|z}z~zLtaAbAcAdAeAfAgAhAiA0mjAytOtkAiilAQwRwSwTwUwVwWwXwYwZw0w1w2w3w4w5w6w7w8w9w!w#w$w%w'w(w)w*w+w,w-w.w/w:w;w=w?w@w[w]w^wPt$N%N'N(N)N*N+N,N-N.N/N% :NXd{q;jk8l8m8n8o8p8=j;NQt=NRt*gq8r8s8t8ymzmAmBmCmDm?NEmFmGmHmImStTtJm@N[NUt8hVt9hWt]N^N_Nu8jiv8w8x8y8z8A8B8C8D8E8F8G8H8I8J8K8L8M8N8O8P8Q8R8S8GgztHgAtIgJgKgLgBtMgNgCtOgDtPgQgRgSgTgUgEtFtVgGtWgXgHtYgItZg0g1g2g3g4gJt5g6gKtT8U8V8
146cdef CUresult cuCtxGetFlags(unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
147 return _driver._cuCtxGetFlags(flags)
150cdef CUresult cuCtxSetFlags(unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
151 return _driver._cuCtxSetFlags(flags)
154cdef CUresult cuCtxGetId(CUcontext ctx, unsigned long long* ctxId) except ?CUDA_ERROR_NOT_FOUND nogil:
155 return _driver._cuCtxGetId(ctx, ctxId)
158cdef CUresult cuCtxSynchronize() except ?CUDA_ERROR_NOT_FOUND nogil:
159 return _driver._cuCtxSynchronize()
162cdef CUresult cuCtxSetLimit(CUlimit limit, size_t value) except ?CUDA_ERROR_NOT_FOUND nogil:
163 return _driver._cuCtxSetLimit(limit, value)
166cdef CUresult cuCtxGetLimit(size_t* pvalue, CUlimit limit) except ?CUDA_ERROR_NOT_FOUND nogil:
167 return _driver._cuCtxGetLimit(pvalue, limit)
170cdef CUresult cuCtxGetCacheConfig(CUfunc_cache* pconfig) except ?CUDA_ERROR_NOT_FOUND nogil:
171 return _driver._cuCtxGetCacheConfig(pconfig)
174cdef CUresult cuCtxSetCacheConfig(CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
175 return _driver._cuCtxSetCacheConfig(config)
178cdef CUresult cuCtxGetApiVersion(CUcontext ctx, unsigned int* version) except ?CUDA_ERROR_NOT_FOUND nogil:
179 return _driver._cuCtxGetApiVersion(ctx, version)
182cdef CUresult cuCtxGetStreamPriorityRange(int* leastPriority, int* greatestPriority) except ?CUDA_ERROR_NOT_FOUND nogil:
183 return _driver._cuCtxGetStreamPriorityRange(leastPriority, greatestPriority) 2-b)j.b/b:b;b)g2 QcCbc 6dC Rd.z*jDb1bI 2b+j5 ?c,j? . /zhb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S 7dSdTdUdLe' 2c8d9d4b5b6bSc7b@ [ ] ibTcUcVc@cVd]c* Gb=b3c4cnbHb3 T L 6 jbEbU V W X Y 7 8 9 ?b5c4 M D J K b B Zc0c1c!d#d$dy ^ z A E kbF G Z 0 1 ]b^b_b_ ` { @b[bN ( ) 6c)bWcXcXeYc! +gYe1m2m%d3m4mMtNt,g-g|q}q~qarbr#jH BbSj*q+q,qTj-q.q/q5m`N{NbcUjJbKbobccdcecLbMbNbObPbQb:z;z=z?z@z[z]z{c+ |cNmOmPmQmRmSmFbTmUmVmWmXm/jhi[c!h?q#h$h@q(g%h'h$j(h)h*hKmmA*b# $ p5|N?j+b%j:eTe:jUeVeXtYtcrZtdr0t1terfr2t3t4tgr5thrirjrkrlrmrnrorpr6tqrrrsrtr7turvr8t9t!t#twr$txr%t'tyrzr(t)t*tAr+tBrCrDrErFrGrHrIrJr,tKrLrMrNr-tOrPr.t/t:t;tQr=tRr?t@tSrTr[t]t^tUr_tVrWrXrYrZr0r1r2r3r`t4r5r6r7r{t8r9r|t}tfcRb[qgcYmZm: lbmb'j{v|v}vTs{iyhubulewzhXsAhBhChYs|i}i~iajwdfwxd1fvlZsbjcjgwjwDjZhAb'lnw0h!s1h2h3h#sEjFjGjHjNdowOdpgkq$sIjJjJeKetwuwvwwwxwywBwEw_z`z{z|z}z~zLtaAbAcAdAeAfAgAhAiA0mjAytOtkAiilA% Xd{q;j=j*g,b
186cdef CUresult cuCtxResetPersistingL2Cache() except ?CUDA_ERROR_NOT_FOUND nogil:
187 return _driver._cuCtxResetPersistingL2Cache()
190cdef CUresult cuCtxGetExecAffinity(CUexecAffinityParam* pExecAffinity, CUexecAffinityType type) except ?CUDA_ERROR_NOT_FOUND nogil:
191 return _driver._cuCtxGetExecAffinity(pExecAffinity, type)
194cdef CUresult cuCtxRecordEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
195 return _driver._cuCtxRecordEvent(hCtx, hEvent)
198cdef CUresult cuCtxWaitEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
199 return _driver._cuCtxWaitEvent(hCtx, hEvent)
202cdef CUresult cuCtxAttach(CUcontext* pctx, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
203 return _driver._cuCtxAttach(pctx, flags)
206cdef CUresult cuCtxDetach(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
207 return _driver._cuCtxDetach(ctx)
210cdef CUresult cuCtxGetSharedMemConfig(CUsharedconfig* pConfig) except ?CUDA_ERROR_NOT_FOUND nogil:
211 return _driver._cuCtxGetSharedMemConfig(pConfig)
214cdef CUresult cuCtxSetSharedMemConfig(CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
215 return _driver._cuCtxSetSharedMemConfig(config)
218cdef CUresult cuModuleLoad(CUmodule* module, const char* fname) except ?CUDA_ERROR_NOT_FOUND nogil:
219 return _driver._cuModuleLoad(module, fname)
222cdef CUresult cuModuleLoadData(CUmodule* module, const void* image) except ?CUDA_ERROR_NOT_FOUND nogil:
223 return _driver._cuModuleLoadData(module, image) 2PeQeWjXjYj%gZj0jReSe1j2j3j4j'g5j6j
226cdef CUresult cuModuleLoadDataEx(CUmodule* module, const void* image, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
227 return _driver._cuModuleLoadDataEx(module, image, numOptions, options, optionValues) 2W8
230cdef CUresult cuModuleLoadFatBinary(CUmodule* module, const void* fatCubin) except ?CUDA_ERROR_NOT_FOUND nogil:
231 return _driver._cuModuleLoadFatBinary(module, fatCubin)
234cdef CUresult cuModuleUnload(CUmodule hmod) except ?CUDA_ERROR_NOT_FOUND nogil:
235 return _driver._cuModuleUnload(hmod) 2PeQeWjXjYj%gZj0jReSe1j2j3j4j'g5j6j
238cdef CUresult cuModuleGetLoadingMode(CUmoduleLoadingMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
239 return _driver._cuModuleGetLoadingMode(mode)
242cdef CUresult cuModuleGetFunction(CUfunction* hfunc, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
243 return _driver._cuModuleGetFunction(hfunc, hmod, name) 2PeQeWjXjYj%gZj0jReSe1j2j3j4j'g5j6j
246cdef CUresult cuModuleGetFunctionCount(unsigned int* count, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
247 return _driver._cuModuleGetFunctionCount(count, mod) 2ot
250cdef CUresult cuModuleEnumerateFunctions(CUfunction* functions, unsigned int numFunctions, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
251 return _driver._cuModuleEnumerateFunctions(functions, numFunctions, mod)
254cdef CUresult cuModuleGetGlobal(CUdeviceptr* dptr, size_t* bytes, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
255 return _driver._cuModuleGetGlobal_v2(dptr, bytes, hmod, name) 2%g'g
258cdef CUresult cuLinkCreate(unsigned int numOptions, CUjit_option* options, void** optionValues, CUlinkState* stateOut) except ?CUDA_ERROR_NOT_FOUND nogil:
259 return _driver._cuLinkCreate_v2(numOptions, options, optionValues, stateOut)
262cdef 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:
263 return _driver._cuLinkAddData_v2(state, type, data, size, name, numOptions, options, optionValues)
266cdef CUresult cuLinkAddFile(CUlinkState state, CUjitInputType type, const char* path, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
267 return _driver._cuLinkAddFile_v2(state, type, path, numOptions, options, optionValues)
270cdef CUresult cuLinkComplete(CUlinkState state, void** cubinOut, size_t* sizeOut) except ?CUDA_ERROR_NOT_FOUND nogil:
271 return _driver._cuLinkComplete(state, cubinOut, sizeOut)
274cdef CUresult cuLinkDestroy(CUlinkState state) except ?CUDA_ERROR_NOT_FOUND nogil:
275 return _driver._cuLinkDestroy(state)
278cdef CUresult cuModuleGetTexRef(CUtexref* pTexRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
279 return _driver._cuModuleGetTexRef(pTexRef, hmod, name)
282cdef CUresult cuModuleGetSurfRef(CUsurfref* pSurfRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
283 return _driver._cuModuleGetSurfRef(pSurfRef, hmod, name)
286cdef 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:
287 return _driver._cuLibraryLoadData(library, code, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 22 QcCbc C RdDb1bI 2b5 ?c? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S ' 4b5b6bSc7bVjsm`b)d{b*d|b+d}b,d~b-dac.dMe9b!b#b$b%bT L bt7g6 jbEb(b4 M D J K b y ^ z A E kbF G Z 0 1 N ( ) )bWcXcXeYc! H Bb+ Fb[c/e_n`n+bTe:j+h,h}c-h~c.h/had:h;h=h?h@h[h]h^h_hbd`h{h|h}h~haibicidieicdfi}n~ndtaoetbocodo: eomiftgthtitjtktlt^zmtntotfogohoq5ior5X8Y8Z8lbmbjokolomonooopoqorosotouovowoxoyozoAoBoCoDoEoFoGoHoIoJoKoLoMoNoOoPoQoRoSoToUoVoWoXoYoZo0o1o2o3o4o5o6o7o8o9o!o#o$o%o'o(o)o*o+o,o-o.oic^ocfNs{ojcbpefPsSb@d; lfkcbhpbqbTb| } ~ abrbkdmcmpmfSsUb]k~dqpsbldVbcldesptbncHf@iocphqhiejerhjlJfKfLfMfmdNfklOfPfpcndodpdke'c(cWb)c*c+cqcIpQfWs, bbpltc]i^iWfXf_iLpshthuhMpYfnevhNpwhxhucZfubajwdvlvcZp2f1sXboe= 9fwcvbwbYbcbdbebfbxbBdyc!p!fzc*p$fybCdZbUlzezbAc{fujBcUhVhEeFeWh1l}f~fagbgDdcg2ldgegCcEdFdGdGe-c.c0b/c:c;cDc~pfg- gbGcdqlgHcngAbHjNdIcqqqg's(sJcxqsg*sKcEqug,sLcLqwg.sMcSqyg:sNcZqAg=sOc6qCgPc%qEg]jyx
290cdef 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:
291 return _driver._cuLibraryLoadFromFile(library, fileName, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2s5t5u5v5
294cdef CUresult cuLibraryUnload(CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
295 return _driver._cuLibraryUnload(library)
298cdef CUresult cuLibraryGetKernel(CUkernel* pKernel, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
299 return _driver._cuLibraryGetKernel(pKernel, library, name) 22 QcCbc C RdDb1bI 2b5 ?c? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S ' 4b5b6bSc7bVjsm`b)d{b*d|b+d}b,d~b-dac.dMe9b!b#b$b%bT L bt7g6 jbEb(b4 M D J K b y ^ z A E kbF G Z 0 1 N ( ) )bWcXcXeYc! H Bb+ Fb[c/e_n`n+bTe:j+h,h}c-h~c.h/had:h;h=h?h@h[h]h^h_hbd`h{h|h}h~haibicidieicdfi}n~ndtaoetbocodo: eomiftgthtitjtktlt^zmtntfos5got5hoq5iou5v5r5lbmbjokolomonooopoqorosotouovowoxoyozoAoBoCoDoEoFoGoHoIoJoKoLoMoNoOoPoQoRoSoToUoVoWoXoYoZo0o1o2o3o4o5o6o7o8o9o!o#o$o%o'o(o)o*o+o,o-o.oic^ocf{ojcbpefSb@d; lfkcpbqbTb| } ~ abrbkdmcmpmfUb]k~dsbldVbcldetbncHf@iocphqhiejerhjlJfKfLfMfmdNfklOfPfpcndodpdke'c(cWb)c*c+cqcIpQf, bbtcMpYfucZfubajwdvcZp2fXboe= 9fwcvbwbYbcbdbebfbxbBdyc!p!fzc*p$fybCdZbUlzezbAc{fujBcUhVhEeFeWh1l}f~fagbgDdcg2ldgegCcEdFdGdGe-c.c0b/c:c;cDc~pfg- gbGcdqlgHcngAbHjNdIcqqqgJcxqsgKcEqugLcLqwgMcSqygNcZqAgOc6qCgPc%qEg]jyx
302cdef CUresult cuLibraryGetKernelCount(unsigned int* count, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
303 return _driver._cuLibraryGetKernelCount(count, lib)
306cdef CUresult cuLibraryEnumerateKernels(CUkernel* kernels, unsigned int numKernels, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
307 return _driver._cuLibraryEnumerateKernels(kernels, numKernels, lib)
310cdef CUresult cuLibraryGetModule(CUmodule* pMod, CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
311 return _driver._cuLibraryGetModule(pMod, library) 2ot
314cdef CUresult cuKernelGetFunction(CUfunction* pFunc, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
315 return _driver._cuKernelGetFunction(pFunc, kernel)
318cdef CUresult cuKernelGetLibrary(CUlibrary* pLib, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
319 return _driver._cuKernelGetLibrary(pLib, kernel)
322cdef CUresult cuLibraryGetGlobal(CUdeviceptr* dptr, size_t* bytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
323 return _driver._cuLibraryGetGlobal(dptr, bytes, library, name)
326cdef CUresult cuLibraryGetManaged(CUdeviceptr* dptr, size_t* bytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
327 return _driver._cuLibraryGetManaged(dptr, bytes, library, name)
330cdef CUresult cuLibraryGetUnifiedFunction(void** fptr, CUlibrary library, const char* symbol) except ?CUDA_ERROR_NOT_FOUND nogil:
331 return _driver._cuLibraryGetUnifiedFunction(fptr, library, symbol)
334cdef CUresult cuKernelGetAttribute(int* pi, CUfunction_attribute attrib, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
335 return _driver._cuKernelGetAttribute(pi, attrib, kernel, dev) 2bt7g6 {4dtet|4}4gxhxixjxkxlxmxnxoxpxqxrxsxtxuxvxwxxx~4a5b5c5d5e5f5g5h5i5j5k5l5m5n5o5
338cdef CUresult cuKernelSetAttribute(CUfunction_attribute attrib, int val, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
339 return _driver._cuKernelSetAttribute(attrib, val, kernel, dev)
342cdef CUresult cuKernelSetCacheConfig(CUkernel kernel, CUfunc_cache config, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
343 return _driver._cuKernelSetCacheConfig(kernel, config, dev)
346cdef CUresult cuKernelGetName(const char** name, CUkernel hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
347 return _driver._cuKernelGetName(name, hfunc) 208
350cdef CUresult cuKernelGetParamInfo(CUkernel kernel, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil:
351 return _driver._cuKernelGetParamInfo(kernel, paramIndex, paramOffset, paramSize) 2: miftgthtitjtktlt^zmtnt18
354cdef CUresult cuMemGetInfo(size_t* free, size_t* total) except ?CUDA_ERROR_NOT_FOUND nogil:
355 return _driver._cuMemGetInfo_v2(free, total)
358cdef CUresult cuMemAlloc(CUdeviceptr* dptr, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil:
359 return _driver._cuMemAlloc_v2(dptr, bytesize) 2PeQe#jnAw5Ib~tx5auy5z5A5B5C56m!rbucu#r}N~NaOD5ReSeLmUeVe$z%zXtYtcrZtdr0t1terfr2t3t4tgr5thrirjrkrlrmrnrorpr6tqrrrsrtr7turvr8t9t/g{n`g[qYmZm
362cdef CUresult cuMemAllocPitch(CUdeviceptr* dptr, size_t* pPitch, size_t WidthInBytes, size_t Height, unsigned int ElementSizeBytes) except ?CUDA_ERROR_NOT_FOUND nogil:
363 return _driver._cuMemAllocPitch_v2(dptr, pPitch, WidthInBytes, Height, ElementSizeBytes)
366cdef CUresult cuMemFree(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
367 return _driver._cuMemFree_v2(dptr) 2*eB y ^ z A E kbF G Z 0 1 PeQe+G,G-G.G/Gct:G=G@Gdu]G^G#j`cH bcJbKbobdcec-e.eLbMbNbObPbQb:qnAeuw5Ib~tx5auy5z5A5B5C56m!rbucu#r}N~NaO+b%j:eD5ReSeLmUeVe$z4k%zLs'zXtYtcrZtdr0t1terfr2t3t4tgr5thrirjrkrlrmrnrorpr6tqrrrsrtr7turvr8t9t:t;tQr=tRr?t@tSrTr[t]t^tUr_tVrWrXrYrZr0r1r2r3r`t4r5r6r7r{t8r9r|t}t/gum{n`g[qYmZm
370cdef CUresult cuMemGetAddressRange(CUdeviceptr* pbase, size_t* psize, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
371 return _driver._cuMemGetAddressRange_v2(pbase, psize, dptr)
374cdef CUresult cuMemAllocHost(void** pp, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil:
375 return _driver._cuMemAllocHost_v2(pp, bytesize) 22 c C I . d e f g h i j k l m n o p q r s O t u v w x P Q R S 4 M D J K b 7cN ( ) H Bb+ Fb*b# $ +b+h,h}c-h~c.h/had:h;h=h?h@h[h]h^h_hbd`h{h|h}h~haibicidieicdfiLmUeVext(z)z!t#twr$txr%t'tyrzr(t)t*tAr+tBrCrDrErFrGrHrIrJr,tKrLrMrNr-tOrPr.t/t/g: lbmb
378cdef CUresult cuMemFreeHost(void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
379 return _driver._cuMemFreeHost(p) 22 c C I . d e f g h i j k l m n o p q r s O t u v w x P Q R S 4 M D J K b 7cB N ( ) H E5F5+ Fb*b# $ +b+h,h}c-h~c.h/had:h;h=h?h@h[h]h^h_hbd`h{h|h}h~haibicidieicdfiLmUeVext(z)z!t#twr$txr%t'tyrzr(t)t*tAr+tBrCrDrErFrGrHrIrJr,tKrLrMrNr-tOrPr.t/t/g: lbmb
382cdef CUresult cuMemHostAlloc(void** pp, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
383 return _driver._cuMemHostAlloc(pp, bytesize, Flags) 2E5F5
386cdef CUresult cuMemHostGetDevicePointer(CUdeviceptr* pdptr, void* p, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
387 return _driver._cuMemHostGetDevicePointer_v2(pdptr, p, Flags)
390cdef CUresult cuMemHostGetFlags(unsigned int* pFlags, void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
391 return _driver._cuMemHostGetFlags(pFlags, p)
394cdef CUresult cuMemAllocManaged(CUdeviceptr* dptr, size_t bytesize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
395 return _driver._cuMemAllocManaged(dptr, bytesize, flags) 2y ^ z A E kbF G Z 0 1 *r+r-r/r:rctXnYnZndu=r?rH BbbcUjJbKbobccdcecLbMbNbObPbQb:qeu+b%j:eLmUeVe4kLs'z:t;tQr=tRr?t@tSrTr[t]t^tUr_tVrWrXrYrZr0r1r2r3r`t4r5r6r7r{t8r9r|t}t/gum
398cdef CUresult cuDeviceRegisterAsyncNotification(CUdevice device, CUasyncCallback callbackFunc, void* userData, CUasyncCallbackHandle* callback) except ?CUDA_ERROR_NOT_FOUND nogil:
399 return _driver._cuDeviceRegisterAsyncNotification(device, callbackFunc, userData, callback)
402cdef CUresult cuDeviceUnregisterAsyncNotification(CUdevice device, CUasyncCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
403 return _driver._cuDeviceUnregisterAsyncNotification(device, callback)
406cdef CUresult cuDeviceGetByPCIBusId(CUdevice* dev, const char* pciBusId) except ?CUDA_ERROR_NOT_FOUND nogil:
407 return _driver._cuDeviceGetByPCIBusId(dev, pciBusId)
410cdef CUresult cuDeviceGetPCIBusId(char* pciBusId, int len, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
411 return _driver._cuDeviceGetPCIBusId(pciBusId, len, dev)
414cdef CUresult cuIpcGetEventHandle(CUipcEventHandle* pHandle, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
415 return _driver._cuIpcGetEventHandle(pHandle, event) 2H BbSj*q+q,qTj-q.q/q5m'jJeKe
418cdef CUresult cuIpcOpenEventHandle(CUevent* phEvent, CUipcEventHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
419 return _driver._cuIpcOpenEventHandle(phEvent, handle)
422cdef CUresult cuIpcGetMemHandle(CUipcMemHandle* pHandle, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
423 return _driver._cuIpcGetMemHandle(pHandle, dptr)
426cdef CUresult cuIpcOpenMemHandle(CUdeviceptr* pdptr, CUipcMemHandle handle, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
427 return _driver._cuIpcOpenMemHandle_v2(pdptr, handle, Flags)
430cdef CUresult cuIpcCloseMemHandle(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
431 return _driver._cuIpcCloseMemHandle(dptr)
434cdef CUresult cuMemHostRegister(void* p, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
435 return _driver._cuMemHostRegister_v2(p, bytesize, Flags) 2*z+z
438cdef CUresult cuMemHostUnregister(void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
439 return _driver._cuMemHostUnregister(p) 2*z+z
442cdef CUresult cuMemcpy(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
443 return _driver._cuMemcpy(dst, src, ByteCount)
446cdef CUresult cuMemcpyPeer(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
447 return _driver._cuMemcpyPeer(dstDevice, dstContext, srcDevice, srcContext, ByteCount)
450cdef CUresult cuMemcpyHtoD(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
451 return _driver._cuMemcpyHtoD_v2(dstDevice, srcHost, ByteCount) 2nAIb}N~NaO
454cdef CUresult cuMemcpyDtoH(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
455 return _driver._cuMemcpyDtoH_v2(dstHost, srcDevice, ByteCount) 2@ [ ] ibT L U V W X Y 7 8 9 nAIb
458cdef CUresult cuMemcpyDtoD(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
459 return _driver._cuMemcpyDtoD_v2(dstDevice, srcDevice, ByteCount)
462cdef CUresult cuMemcpyDtoA(CUarray dstArray, size_t dstOffset, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
463 return _driver._cuMemcpyDtoA_v2(dstArray, dstOffset, srcDevice, ByteCount)
466cdef CUresult cuMemcpyAtoD(CUdeviceptr dstDevice, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
467 return _driver._cuMemcpyAtoD_v2(dstDevice, srcArray, srcOffset, ByteCount)
470cdef CUresult cuMemcpyHtoA(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
471 return _driver._cuMemcpyHtoA_v2(dstArray, dstOffset, srcHost, ByteCount)
474cdef CUresult cuMemcpyAtoH(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
475 return _driver._cuMemcpyAtoH_v2(dstHost, srcArray, srcOffset, ByteCount)
478cdef CUresult cuMemcpyAtoA(CUarray dstArray, size_t dstOffset, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
479 return _driver._cuMemcpyAtoA_v2(dstArray, dstOffset, srcArray, srcOffset, ByteCount)
482cdef CUresult cuMemcpy2D(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
483 return _driver._cuMemcpy2D_v2(pCopy)
486cdef CUresult cuMemcpy2DUnaligned(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
487 return _driver._cuMemcpy2DUnaligned_v2(pCopy)
490cdef CUresult cuMemcpy3D(const CUDA_MEMCPY3D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
491 return _driver._cuMemcpy3D_v2(pCopy)
494cdef CUresult cuMemcpy3DPeer(const CUDA_MEMCPY3D_PEER* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
495 return _driver._cuMemcpy3DPeer(pCopy)
498cdef CUresult cuMemcpyAsync(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
499 return _driver._cuMemcpyAsync(dst, src, ByteCount, hStream) 2y ^ z A E kbF G Z 0 1 H BbbcUjJbKbobccdcecLbMbNbObPbQb*b# $ +b%j:eUeVefcRbgc: lbmb
502cdef CUresult cuMemcpyPeerAsync(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
503 return _driver._cuMemcpyPeerAsync(dstDevice, dstContext, srcDevice, srcContext, ByteCount, hStream)
506cdef CUresult cuMemcpyHtoDAsync(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
507 return _driver._cuMemcpyHtoDAsync_v2(dstDevice, srcHost, ByteCount, hStream) 2~tau6mbucu#r
510cdef CUresult cuMemcpyDtoHAsync(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
511 return _driver._cuMemcpyDtoHAsync_v2(dstHost, srcDevice, ByteCount, hStream) 2PeQe%g~tau6m!rbucuReSe'g
514cdef CUresult cuMemcpyDtoDAsync(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
515 return _driver._cuMemcpyDtoDAsync_v2(dstDevice, srcDevice, ByteCount, hStream)
518cdef CUresult cuMemcpyHtoAAsync(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
519 return _driver._cuMemcpyHtoAAsync_v2(dstArray, dstOffset, srcHost, ByteCount, hStream)
522cdef CUresult cuMemcpyAtoHAsync(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
523 return _driver._cuMemcpyAtoHAsync_v2(dstHost, srcArray, srcOffset, ByteCount, hStream)
526cdef CUresult cuMemcpy2DAsync(const CUDA_MEMCPY2D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
527 return _driver._cuMemcpy2DAsync_v2(pCopy, hStream)
530cdef CUresult cuMemcpy3DAsync(const CUDA_MEMCPY3D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
531 return _driver._cuMemcpy3DAsync_v2(pCopy, hStream) 2% ;j=j*g
534cdef CUresult cuMemcpy3DPeerAsync(const CUDA_MEMCPY3D_PEER* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
535 return _driver._cuMemcpy3DPeerAsync(pCopy, hStream)
538cdef CUresult cuMemsetD8(CUdeviceptr dstDevice, unsigned char uc, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
539 return _driver._cuMemsetD8_v2(dstDevice, uc, N)
542cdef CUresult cuMemsetD16(CUdeviceptr dstDevice, unsigned short us, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
543 return _driver._cuMemsetD16_v2(dstDevice, us, N)
546cdef CUresult cuMemsetD32(CUdeviceptr dstDevice, unsigned int ui, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
547 return _driver._cuMemsetD32_v2(dstDevice, ui, N)
550cdef CUresult cuMemsetD2D8(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
551 return _driver._cuMemsetD2D8_v2(dstDevice, dstPitch, uc, Width, Height)
554cdef CUresult cuMemsetD2D16(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
555 return _driver._cuMemsetD2D16_v2(dstDevice, dstPitch, us, Width, Height)
558cdef CUresult cuMemsetD2D32(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
559 return _driver._cuMemsetD2D32_v2(dstDevice, dstPitch, ui, Width, Height)
562cdef CUresult cuMemsetD8Async(CUdeviceptr dstDevice, unsigned char uc, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
563 return _driver._cuMemsetD8Async(dstDevice, uc, N, hStream) 2T L U V W X Y y ^ z A crfrhrirjrqrrrwrzrBrCrDrKrLrQrTrVrWrXr4r5r
566cdef CUresult cuMemsetD16Async(CUdeviceptr dstDevice, unsigned short us, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
567 return _driver._cuMemsetD16Async(dstDevice, us, N, hStream) 2drkrlrmrsrtrxrErFrGrMrNrRrYrZr0r6r7r
570cdef CUresult cuMemsetD32Async(CUdeviceptr dstDevice, unsigned int ui, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
571 return _driver._cuMemsetD32Async(dstDevice, ui, N, hStream) 2ergrnrorprurvryrArHrIrJrOrPrSrUr1r2r3r8r9r
574cdef CUresult cuMemsetD2D8Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
575 return _driver._cuMemsetD2D8Async(dstDevice, dstPitch, uc, Width, Height, hStream)
578cdef CUresult cuMemsetD2D16Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
579 return _driver._cuMemsetD2D16Async(dstDevice, dstPitch, us, Width, Height, hStream)
582cdef CUresult cuMemsetD2D32Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
583 return _driver._cuMemsetD2D32Async(dstDevice, dstPitch, ui, Width, Height, hStream)
586cdef CUresult cuArrayCreate(CUarray* pHandle, const CUDA_ARRAY_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
587 return _driver._cuArrayCreate_v2(pHandle, pAllocateArray) 2G5
590cdef CUresult cuArrayGetDescriptor(CUDA_ARRAY_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
591 return _driver._cuArrayGetDescriptor_v2(pArrayDescriptor, hArray)
594cdef CUresult cuArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUarray array) except ?CUDA_ERROR_NOT_FOUND nogil:
595 return _driver._cuArrayGetSparseProperties(sparseProperties, array)
598cdef CUresult cuMipmappedArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUmipmappedArray mipmap) except ?CUDA_ERROR_NOT_FOUND nogil:
599 return _driver._cuMipmappedArrayGetSparseProperties(sparseProperties, mipmap)
602cdef CUresult cuArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUarray array, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
603 return _driver._cuArrayGetMemoryRequirements(memoryRequirements, array, device)
606cdef CUresult cuMipmappedArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUmipmappedArray mipmap, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
607 return _driver._cuMipmappedArrayGetMemoryRequirements(memoryRequirements, mipmap, device)
610cdef CUresult cuArrayGetPlane(CUarray* pPlaneArray, CUarray hArray, unsigned int planeIdx) except ?CUDA_ERROR_NOT_FOUND nogil:
611 return _driver._cuArrayGetPlane(pPlaneArray, hArray, planeIdx)
614cdef CUresult cuArrayDestroy(CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
615 return _driver._cuArrayDestroy(hArray) 2G5Pt$N%N'N(N)N*N+N,N-N.N/N% :NXd{q;j=jStTt[NUtWt]N^N_Nji
618cdef CUresult cuArray3DCreate(CUarray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
619 return _driver._cuArray3DCreate_v2(pHandle, pAllocateArray) 2Pt$N%N'N(N)N*N+N,N-N.N/N% :NXd{q;j=jStTt[NUtWt]N^N_Nji
622cdef CUresult cuArray3DGetDescriptor(CUDA_ARRAY3D_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
623 return _driver._cuArray3DGetDescriptor_v2(pArrayDescriptor, hArray) 2QtRt*g
626cdef CUresult cuMipmappedArrayCreate(CUmipmappedArray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc, unsigned int numMipmapLevels) except ?CUDA_ERROR_NOT_FOUND nogil:
627 return _driver._cuMipmappedArrayCreate(pHandle, pMipmappedArrayDesc, numMipmapLevels) 2;NQt=NRt*g?N@NVtji
630cdef CUresult cuMipmappedArrayGetLevel(CUarray* pLevelArray, CUmipmappedArray hMipmappedArray, unsigned int level) except ?CUDA_ERROR_NOT_FOUND nogil:
631 return _driver._cuMipmappedArrayGetLevel(pLevelArray, hMipmappedArray, level) 2QtRt*g
634cdef CUresult cuMipmappedArrayDestroy(CUmipmappedArray hMipmappedArray) except ?CUDA_ERROR_NOT_FOUND nogil:
635 return _driver._cuMipmappedArrayDestroy(hMipmappedArray) 2;NQt=NRt*g?N@NVtji
638cdef CUresult cuMemGetHandleForAddressRange(void* handle, CUdeviceptr dptr, size_t size, CUmemRangeHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
639 return _driver._cuMemGetHandleForAddressRange(handle, dptr, size, handleType, flags)
642cdef CUresult cuMemBatchDecompressAsync(CUmemDecompressParams* paramsArray, size_t count, unsigned int flags, size_t* errorIndex, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
643 return _driver._cuMemBatchDecompressAsync(paramsArray, count, flags, errorIndex, stream)
646cdef CUresult cuMemAddressReserve(CUdeviceptr* ptr, size_t size, size_t alignment, CUdeviceptr addr, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
647 return _driver._cuMemAddressReserve(ptr, size, alignment, addr, flags) 2WeWd8chc
650cdef CUresult cuMemAddressFree(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
651 return _driver._cuMemAddressFree(ptr, size) 2WeWd8chc
654cdef CUresult cuMemCreate(CUmemGenericAllocationHandle* handle, size_t size, const CUmemAllocationProp* prop, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
655 return _driver._cuMemCreate(handle, size, prop, flags) 2WeWd8chc
658cdef CUresult cuMemRelease(CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
659 return _driver._cuMemRelease(handle) 2WeWd8chc
662cdef CUresult cuMemMap(CUdeviceptr ptr, size_t size, size_t offset, CUmemGenericAllocationHandle handle, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
663 return _driver._cuMemMap(ptr, size, offset, handle, flags) 2WeWd8chc
666cdef CUresult cuMemMapArrayAsync(CUarrayMapInfo* mapInfoList, unsigned int count, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
667 return _driver._cuMemMapArrayAsync(mapInfoList, count, hStream)
670cdef CUresult cuMemUnmap(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
671 return _driver._cuMemUnmap(ptr, size) 2WeWd8chc
674cdef CUresult cuMemSetAccess(CUdeviceptr ptr, size_t size, const CUmemAccessDesc* desc, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
675 return _driver._cuMemSetAccess(ptr, size, desc, count) 2WeWd8chc
678cdef CUresult cuMemGetAccess(unsigned long long* flags, const CUmemLocation* location, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
679 return _driver._cuMemGetAccess(flags, location, ptr)
682cdef CUresult cuMemExportToShareableHandle(void* shareableHandle, CUmemGenericAllocationHandle handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
683 return _driver._cuMemExportToShareableHandle(shareableHandle, handle, handleType, flags)
686cdef CUresult cuMemImportFromShareableHandle(CUmemGenericAllocationHandle* handle, void* osHandle, CUmemAllocationHandleType shHandleType) except ?CUDA_ERROR_NOT_FOUND nogil:
687 return _driver._cuMemImportFromShareableHandle(handle, osHandle, shHandleType)
690cdef CUresult cuMemGetAllocationGranularity(size_t* granularity, const CUmemAllocationProp* prop, CUmemAllocationGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil:
691 return _driver._cuMemGetAllocationGranularity(granularity, prop, option) 2WeWd8chc
694cdef CUresult cuMemGetAllocationPropertiesFromHandle(CUmemAllocationProp* prop, CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
695 return _driver._cuMemGetAllocationPropertiesFromHandle(prop, handle)
698cdef CUresult cuMemRetainAllocationHandle(CUmemGenericAllocationHandle* handle, void* addr) except ?CUDA_ERROR_NOT_FOUND nogil:
699 return _driver._cuMemRetainAllocationHandle(handle, addr) 2WeWd8chc
702cdef CUresult cuMemFreeAsync(CUdeviceptr dptr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
703 return _driver._cuMemFreeAsync(dptr, hStream) 2*e8b/ 3 T L 'b8g9gU V !gX Y 7 8 #g$g9 B Zc0c1c!d#d$dy ^ z A E kbF G Z 0 1 ]b^b_b_ ` { +gYebO;G%d?G[G,g-g|q}q~qarbr`c+e,eH .goApAqArAsAtAuAvAwAxAyAzAMibcJbKbobccdcec-eNi.eOiLbMbNbObPbQb4h5h*b# $ 6h7j;e8jfcddvmRb9j/dwm?e9c_e!cedfd:d#c;d$cbfgd=d6k`g7h!jxmgc%c?d: lbmbeHvHyHSxTxUxVxptqtWxXxYxZx0xZH1x0H2x3x1H4x5x6x.HaI+xCy7JWyXyYyZyttut0y1y2y3y4y|J5y}J6y7y~J8y9y!ytKJK/yGzPdQdfMxMPM7M=MgNyNQN% XdymzmAmBmCmDmEmFmGmHmImJm8h9h$rGgztHgAtIgJgKgLgBtMgNgCtOgDtPgQgRgSgTgUgEtFtVgGtWgXgHtYgItZg0g1g2g3g4gJt5g6gKt;q=q,b
706cdef CUresult cuMemAllocAsync(CUdeviceptr* dptr, size_t bytesize, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
707 return _driver._cuMemAllocAsync(dptr, bytesize, hStream) 2!d#d$dy z A E F G Z 0 1 ]b^b_b_ ` {
710cdef CUresult cuMemPoolTrimTo(CUmemoryPool pool, size_t minBytesToKeep) except ?CUDA_ERROR_NOT_FOUND nogil:
711 return _driver._cuMemPoolTrimTo(pool, minBytesToKeep)
714cdef CUresult cuMemPoolSetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
715 return _driver._cuMemPoolSetAttribute(pool, attr, value) 2AA6h
718cdef CUresult cuMemPoolGetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
719 return _driver._cuMemPoolGetAttribute(pool, attr, value) 28b/ 3 T L 'b8g9gU V W !gX Y 7 8 #g$g9 Zc0c1cy ^ z A E kbF G AA4h5h*b# $ 6h7j;e8jiC$E9jSi=e?e9cTi@eUi[eVi]e5k^e_e!cWi:g;ged=g?g@g[gfd]gXi`e:d#cYi{eZi|e0i}e1i~e;d$c2iaf^g_g3ibfgd=d7h: lbmb7k$k%kjf; kf[dhdid]d9i^d_d`dlfkc,klcjdbh!i{d|d-k'i-iyhwl7f= 8fpeydzdqefjresete9fwcClxcAdgjhjueveDlIlnjZh(l-l=l^l}ldmimnm% XdymzmAmBmCmDmEmFmGmHmImJm8h9hGgHgIgJgKgLgMgNgOgPgQgRgSgTgUgVgWgXgYgZg0g1g2g3g4g5g6g;q=q,b
722cdef CUresult cuMemPoolSetAccess(CUmemoryPool pool, const CUmemAccessDesc* map, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
723 return _driver._cuMemPoolSetAccess(pool, map, count) 2*eB |r}r~r`cascsdsesfs+egs,ehsisjsH .gkslsmsnsospsqsrssstsusvswsxsyszsAsBsCsDsEsFsGsHsIsJsMibcJbKbobccdcec-eNi.eOiLbMbNbObPbQbfc,vddPiQiRiRb/dSi=e?e9cTi@eUi[eVi]e5k^e_e!cWi:g;ged=g?g@g[gfd]gXi`e:d#cYi{eZi|e0i}e1i~e;d$c2iaf^g_g3ibfgd=d6k`ggc%c?d|n4i5i/o:o;o=oPdQd
726cdef CUresult cuMemPoolGetAccess(CUmemAccess_flags* flags, CUmemoryPool memPool, CUmemLocation* location) except ?CUDA_ERROR_NOT_FOUND nogil:
727 return _driver._cuMemPoolGetAccess(flags, memPool, location) 2$E
730cdef CUresult cuMemPoolCreate(CUmemoryPool* pool, const CUmemPoolProps* poolProps) except ?CUDA_ERROR_NOT_FOUND nogil:
731 return _driver._cuMemPoolCreate(pool, poolProps) 20nuk)q1n`cvk2nwk3nxk+e4n,eyk5nzk6nAk8nBk9nCk!n#n$n%n'n(n)n*n+n,n-n.nDkEkFkGkHkIkJkKkLkMkNkOk/nPk:nni;nQk=nRk?nSkobcc@nTk[nUk]nVkLbMbNbObPbQbAAfc,vddPiQiRiRb/dSi=e?e9cTi@eUi[eVi]e5k^e_e!cWi:g;ged=g?g@g[gfd]gXi`e:d#cYi{eZi|e0i}e1i~e;d$c2iaf^g_g3ibfgd=d6kgc%c?d|n4i5i/o:o;o=oPdQd
734cdef CUresult cuMemPoolDestroy(CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
735 return _driver._cuMemPoolDestroy(pool) 2*eB |r}r~r`cascsdsesfs+egs,ehsisjsH .gkslsmsnsospsqsrssstsusvswsxsyszsAsBsCsDsEsFsGsHsIsJsMibcJbKbobccdcec-eNi.eOiLbMbNbObPbQbAAfc,vddPiQiRiRb/dSi=e?e9cTi@eUi[eVi]e5k^e_e!cWi:g;ged=g?g@g[gfd]gXi`e:d#cYi{eZi|e0i}e1i~e;d$c2iaf^g_g3ibfgd=d6k`ggc%c?d|n4i5i/o:o;o=oPdQd
738cdef CUresult cuMemAllocFromPoolAsync(CUdeviceptr* dptr, size_t bytesize, CUmemoryPool pool, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
739 return _driver._cuMemAllocFromPoolAsync(dptr, bytesize, pool, hStream) 28b/ 3 T L 'b8g9gU V W !gX Y 7 8 #g$g9 Zc0c1cy ^ z A E kbF G +gYebOrk%dsktk,g-g|q}q~qarbr)q`cbs_w`w{w+e,eH Bb7n.goApAqArAsAtAuAvAwAxAyAzAKs|w}w~wMiaxbcUjJbKbobccdcec-eNi.eOiLbMbNbObPbQb4h5h*b# $ 6h7j;e8jfcddvmRb9j/dwm?e9c_e!cedfd:d#c;d$cbfgd=d6k7h!jxmgc%c?d: lbmb7k$k%kjf; kf[dhdid]d9i^d_d`dlfkc,klcjdbh!i{d|d-k'i-iyhwl7f= 8fpeydzdqefjresete9fwcClxcAdgjhjueveDlIlnjZhPdQd(l-l=l^l}ldmimnm% XdymzmAmBmCmDmEmFmGmHmImJm8h9h$rGgztHgAtIgJgKgLgBtMgNgCtOgDtPgQgRgSgTgUgEtFtVgGtWgXgHtYgItZg0g1g2g3g4gJt5g6gKt;q=q,b
742cdef CUresult cuMemPoolExportToShareableHandle(void* handle_out, CUmemoryPool pool, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
743 return _driver._cuMemPoolExportToShareableHandle(handle_out, pool, handleType, flags) 20nuk)q1n`cvk2nwk3nxk+e4n,eyk5nzk6nAk8nBk9nCk!n#n$n%n'n(n)n*n+n,n-n.nDkEkFkGkHkIkJkKkLkMkNkOk/nPk:nni;nQk=nRk?nSkobcc@nTk[nUk]nVkLbMbNbObPbQb=e9c@e[e]e^e!c:g`e#c{e|e}e~e$caf%c4i5i/o:o;o=oPdQd
746cdef CUresult cuMemPoolImportFromShareableHandle(CUmemoryPool* pool_out, void* handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
747 return _driver._cuMemPoolImportFromShareableHandle(pool_out, handle, handleType, flags)
750cdef CUresult cuMemPoolExportPointer(CUmemPoolPtrExportData* shareData_out, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
751 return _driver._cuMemPoolExportPointer(shareData_out, ptr) 2)q`cbs_w`w{w+e,eH Bb7n.goApAqArAsAtAuAvAwAxAyAzAKs|w}w~wMiaxbcUjJbKbobccdcec-eNi.eOiLbMbNbObPbQb%cPdQd
754cdef CUresult cuMemPoolImportPointer(CUdeviceptr* ptr_out, CUmemoryPool pool, CUmemPoolPtrExportData* shareData) except ?CUDA_ERROR_NOT_FOUND nogil:
755 return _driver._cuMemPoolImportPointer(ptr_out, pool, shareData)
758cdef CUresult cuMulticastCreate(CUmemGenericAllocationHandle* mcHandle, const CUmulticastObjectProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
759 return _driver._cuMulticastCreate(mcHandle, prop)
762cdef CUresult cuMulticastAddDevice(CUmemGenericAllocationHandle mcHandle, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
763 return _driver._cuMulticastAddDevice(mcHandle, dev)
766cdef 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:
767 return _driver._cuMulticastBindMem(mcHandle, mcOffset, memHandle, memOffset, size, flags)
770cdef CUresult cuMulticastBindAddr(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
771 return _driver._cuMulticastBindAddr(mcHandle, mcOffset, memptr, size, flags)
774cdef CUresult cuMulticastUnbind(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
775 return _driver._cuMulticastUnbind(mcHandle, dev, mcOffset, size)
778cdef CUresult cuMulticastGetGranularity(size_t* granularity, const CUmulticastObjectProp* prop, CUmulticastGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil:
779 return _driver._cuMulticastGetGranularity(granularity, prop, option)
782cdef CUresult cuPointerGetAttribute(void* data, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
783 return _driver._cuPointerGetAttribute(data, attribute, ptr) 2@ [ ] ib1e4e7e!e%e)e8b/ 3 'bU V W X Y eudfffiflc}dnfaerfeeheIfmdWbRf, rcsc,cqdrdsdtdmene0fxd3f6fxcwe#f%f*fAeDe|fDd0bgg- EcFc=cHdIdJdKdIemgogOdrgtgvgxgzgBgDgFg$r,b
786cdef CUresult cuMemPrefetchAsync(CUdeviceptr devPtr, size_t count, CUmemLocation location, unsigned int flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
787 return _driver._cuMemPrefetchAsync_v2(devPtr, count, location, flags, hStream) 21m2m%d3m4m
790cdef CUresult cuMemAdvise(CUdeviceptr devPtr, size_t count, CUmem_advise advice, CUmemLocation location) except ?CUDA_ERROR_NOT_FOUND nogil:
791 return _driver._cuMemAdvise_v2(devPtr, count, advice, location) 2PuWn,r.rH5ducOdO:q
794cdef CUresult cuMemRangeGetAttribute(void* data, size_t dataSize, CUmem_range_attribute attribute, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
795 return _driver._cuMemRangeGetAttribute(data, dataSize, attribute, devPtr, count) 2YePuWn,r.r%d3m4mducOdO,g-g:q
798cdef 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:
799 return _driver._cuMemRangeGetAttributes(data, dataSizes, attributes, numAttributes, devPtr, count) 2:q
802cdef CUresult cuPointerSetAttribute(const void* value, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
803 return _driver._cuPointerSetAttribute(value, attribute, ptr) 2eu
806cdef CUresult cuPointerGetAttributes(unsigned int numAttributes, CUpointer_attribute* attributes, void** data, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
807 return _driver._cuPointerGetAttributes(numAttributes, attributes, data, ptr) 22 c C I . d e f g h i j k l m n o p q r s O t u v w x P Q R S 4 M D J K b 7cN ( ) +gYePuWn,r.rH51m2m%d3m4mMtNtducOdO,g-g#jeu28*b# $ +h,h}c-h~c.h/had:h;h=h?h@h[h]h^h_hbd`h{h|h}h~haibicidieicdfixt4k6h7j38Ls'z(z)z*z+zumdd7h!j: lbmb$r485868788898!8#8$8%8
810cdef CUresult cuStreamCreate(CUstream* phStream, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
811 return _driver._cuStreamCreate(phStream, Flags) 2PeQeWjXjYj%gZj0j@jeOkiIb6m!r#rI5ReSe1j2j3j4j'g5j6j
814cdef CUresult cuStreamCreateWithPriority(CUstream* phStream, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil:
815 return _driver._cuStreamCreateWithPriority(phStream, flags, priority) 2-b)j.b/b:b;b)g2 QcCbc 6dC Rd.z*jDb1bI 2b+j5 ?c,j? . /zhb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S 7dSdTdUdLe' 2c8d9d4b5b6bSc7b@ [ ] ibTcUcVc@cVd]c* Gb=b3c4cnbHb3 T L 6 jbEbU V W X Y 7 8 9 ?b5c4 M D J K b B Zc0c1c!d#d$dy ^ z A E kbF G Z 0 1 ]b^b_b_ ` { @b[bN ( ) 6c)bWcXcXeYc! +gYe1m2m%d3m4mMtNt,g-g|q}q~qarbr#jH BbSj*q+q,qTj-q.q/q5m`N{NbcUjJbKbobccdcecLbMbNbObPbQb:z;z=z?z@z[z]z{c+ |cNmOmPmQmRmSmFbTmUmVmWmXm/jhi[c!h?q#h$h@q(g%h'h$j(h)h*hKm+b%j:eTe:jUeVeXtYtcrZtdr0t1terfr2t3t4tgr5thrirjrkrlrmrnrorpr6tqrrrsrtr7turvr8t9t!t#twr$txr%t'tyrzr(t)t*tAr+tBrCrDrErFrGrHrIrJr,tKrLrMrNr-tOrPr.t/t:t;tQr=tRr?t@tSrTr[t]t^tUr_tVrWrXrYrZr0r1r2r3r`t4r5r6r7r{t8r9r|t}tfcRb[qgcYmZm: lbmb'j{v|v}vTs{iyhubulewzhXsAhBhChYs|i}i~iajwdfwxd1fvlZsbjcjgwjwDjZhAb'lnw0h!s1h2h3h#sEjFjGjHjNdowOdpgkq$sIjJjJeKetwuwvwwwxwywBwEw_z`z{z|z}z~zLtaAbAcAdAeAfAgAhAiA0mjAytOtkAiilA% Xd{q;j=j*g,b
818cdef CUresult cuStreamGetPriority(CUstream hStream, int* priority) except ?CUDA_ERROR_NOT_FOUND nogil:
819 return _driver._cuStreamGetPriority(hStream, priority)
822cdef CUresult cuStreamGetDevice(CUstream hStream, CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil:
823 return _driver._cuStreamGetDevice(hStream, device)
826cdef CUresult cuStreamGetFlags(CUstream hStream, unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
827 return _driver._cuStreamGetFlags(hStream, flags)
830cdef CUresult cuStreamGetId(CUstream hStream, unsigned long long* streamId) except ?CUDA_ERROR_NOT_FOUND nogil:
831 return _driver._cuStreamGetId(hStream, streamId)
834cdef CUresult cuStreamGetCtx(CUstream hStream, CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
835 return _driver._cuStreamGetCtx(hStream, pctx)
838cdef CUresult cuStreamGetCtx_v2(CUstream hStream, CUcontext* pCtx, CUgreenCtx* pGreenCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
839 return _driver._cuStreamGetCtx_v2(hStream, pCtx, pGreenCtx)
842cdef CUresult cuStreamWaitEvent(CUstream hStream, CUevent hEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
843 return _driver._cuStreamWaitEvent(hStream, hEvent, Flags) 2CbDb5 ? d e f g h i j k l m n o p q r s t u v w x ! ii,b
846cdef CUresult cuStreamAddCallback(CUstream hStream, CUstreamCallback callback, void* userData, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
847 return _driver._cuStreamAddCallback(hStream, callback, userData, flags)
850cdef CUresult cuStreamBeginCapture(CUstream hStream, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil:
851 return _driver._cuStreamBeginCapture_v2(hStream, mode) 2-b)j.b/b:b;b)g2 QcCbc 6dC Rd*jDb1bI 2b+j5 ?c,j? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S * Zc0c1c!d#d$dy z A E F G Z 0 1 ]b^b_b_ ` { N ( )bWcXcXeYc! %
854cdef CUresult cuStreamBeginCaptureToGraph(CUstream hStream, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil:
855 return _driver._cuStreamBeginCaptureToGraph(hStream, hGraph, dependencies, dependencyData, numDependencies, mode) 2c 6dd e f g h i j k l m n o p q r s O t u v w x P Q R S N !
858cdef CUresult cuThreadExchangeStreamCaptureMode(CUstreamCaptureMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
859 return _driver._cuThreadExchangeStreamCaptureMode(mode)
862cdef CUresult cuStreamEndCapture(CUstream hStream, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
863 return _driver._cuStreamEndCapture(hStream, phGraph) 2-b)j.b/b:b;b)g2 QcCbc 6dC Rd*jDb1bI 2b+j5 ?c,j? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S * Zc0c1c!d#d$dy z A E F G Z 0 1 ]b^b_b_ ` { N ( )bWcXcXeYc! %
866cdef CUresult cuStreamIsCapturing(CUstream hStream, CUstreamCaptureStatus* captureStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
867 return _driver._cuStreamIsCapturing(hStream, captureStatus) 28b/ 3 T L 'b8g9gU V W !gX Y 7 8 #g$g9 Zc0c1c!d#d$dy ^ z A E kbF G Z 0 1 ]b^b_b_ ` { +gYebOrk%dsktk,g-g|q}q~qarbr)q`cbs_w`w{w+e,eH Bb7n.goApAqArAsAtAuAvAwAxAyAzAKs|w}w~wMiaxbcUjJbKbobccdcec-eNi.eOiLbMbNbObPbQb4h5h*b# $ 6h7j;e8jfcddvmRb9j/dwm?e9c_e!cedfd:d#c;d$cbfgd=d6k7h!jxmgc%c?d: lbmb7k$k%kjf; kf[dhdid]d9i^d_d`dlfkc,klcjdbh!i{d|d-k'i-iyhwl7f= 8fpeydzdqefjresete9fwcClxcAdgjhjueveDlIlnjZhPdQd(l-l=l^l}ldmimnm% XdymzmAmBmCmDmEmFmGmHmImJm8h9h$rGgztHgAtIgJgKgLgBtMgNgCtOgDtPgQgRgSgTgUgEtFtVgGtWgXgHtYgItZg0g1g2g3g4gJt5g6gKt;q=q,b
870cdef CUresult cuStreamGetCaptureInfo_v2(CUstream hStream, CUstreamCaptureStatus* captureStatus_out, cuuint64_t* id_out, CUgraph* graph_out, const CUgraphNode** dependencies_out, size_t* numDependencies_out) except ?CUDA_ERROR_NOT_FOUND nogil:
871 return _driver._cuStreamGetCaptureInfo_v2(hStream, captureStatus_out, id_out, graph_out, dependencies_out, numDependencies_out)
874cdef 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:
875 return _driver._cuStreamGetCaptureInfo_v3(hStream, captureStatus_out, id_out, graph_out, dependencies_out, edgeData_out, numDependencies_out) 2-b)j.b/b:b;b)g2 QcCbc 6dC Rd*jDb1bI 2b+j5 ?c,j? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S * Zc0c1c!d#d$dy z A E F G Z 0 1 ]b^b_b_ ` { N ( )bWcXcXeYc! %
878cdef CUresult cuStreamUpdateCaptureDependencies(CUstream hStream, CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
879 return _driver._cuStreamUpdateCaptureDependencies_v2(hStream, dependencies, dependencyData, numDependencies, flags) 22 c 6dC d e f g h i j k l m n o p q r s O t u v w x P Q R S * N !
882cdef CUresult cuStreamAttachMemAsync(CUstream hStream, CUdeviceptr dptr, size_t length, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
883 return _driver._cuStreamAttachMemAsync(hStream, dptr, length, flags)
886cdef CUresult cuStreamQuery(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
887 return _driver._cuStreamQuery(hStream)
890cdef CUresult cuStreamSynchronize(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
891 return _driver._cuStreamSynchronize(hStream) 2-b.b/b:b;b2 c C I 5 ?c. hb3bd e f g h i j k l m n o p q r s O t u v w x P Q R S 7dSdTdUdLe' 2c8d9d4b5b6bSc7b@ [ ] ibTcUcVc@cVd8b]cGb=b3c4c/ nbHb3 T L 6 jbEb'b8g9gU V W !gX Y 7 8 #g$g9 ?b5c4 M D J K b 7cB y ^ z A E kbF G Z 0 1 ]b^b_b_ ` { @b[bN ( ) 6cPeQeWjXjYj%gZj0j+gYe1m2m%d3m4m,g-gH Ib~tau6m!rbucu#r{c+ |cFb*b# $ ?j+bReSe1j2j3j4j'g5j6jTe:j+h,h}c-h~c.h/had:h;h=h?h@h[h]h^h_hbd`h{h|h}h~haibicidieicdfi'8YmZm: lbmbOtii% ;j=j*g$r,b
894cdef CUresult cuStreamDestroy(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
895 return _driver._cuStreamDestroy_v2(hStream) 2-b)j.b/b:b;b)g2 QcCbc 6dC Rd.z*jDb1bI 2b+j5 ?c,j? . /zhb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S 7dSdTdUdLe' 2c8d9d4b5b6bSc7b@ [ ] ibTcUcVc@c*eVd]c* Gb=b3c4cnbHb3 T L 6 jbEbU V W X Y 7 8 9 ?b5c4 M D J K b B Zc0c1c!d#d$dy ^ z A E kbF G Z 0 1 ]b^b_b_ ` { @b[bN ( ) 6c)bWcXcXeYc! PeQeWjXjYj%gZj0j+gYe1m2m%d3m4mMtNt,g-g|q}q~qarbr#j`cH SjTj5m`N{NbcJbKbobdcec-e.eLbMbNbObPbQb:z;z=z?z@z[z@jeOkiIb6m!r#r]z{c+ |cNmOmPmQmRmSmFbTmUmVmWmXm/jhi[c!h#h$h@q(g%h'h(h)h*hBAmA*b# $ |N?j+b%j:eI5ReSe1j2j3j4j'g5j6jTe:jUeVeXtYtcrZtdr0t1terfr2t3t4tgr5thrirjrkrlrmrnrorpr6tqrrrsrtr7turvr8t9t!t#twr$txr%t'tyrzr(t)t*tAr+tBrCrDrErFrGrHrIrJr,tKrLrMrNr-tOrPr.t/t:t;tQr=tRr?t@tSrTr[t]t^tUr_tVrWrXrYrZr0r1r2r3r`t4r5r6r7r{t8r9r|t}tfcRb8N`ggcYmZm: lbmb'jsHwHMHoIByCyDyEy1JFyGyrtstHyIyJyKyLy2JMy3JNyOy4JPyQyRy.JXKFzGzHzIz~LJzKzvtwtLzMzNzOzPzaMQzbMRzSzcMTzUzVzJeKetMLM3M.McNuNMN4N_z`z{z|z}z~zLtaAbAcAdAeAfAgAhAiA0mjAytOtkAiilA% Xd{q;j=j*g,b
898cdef CUresult cuStreamCopyAttributes(CUstream dst, CUstream src) except ?CUDA_ERROR_NOT_FOUND nogil:
899 return _driver._cuStreamCopyAttributes(dst, src)
902cdef CUresult cuStreamGetAttribute(CUstream hStream, CUstreamAttrID attr, CUstreamAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
903 return _driver._cuStreamGetAttribute(hStream, attr, value_out)
906cdef CUresult cuStreamSetAttribute(CUstream hStream, CUstreamAttrID attr, const CUstreamAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
907 return _driver._cuStreamSetAttribute(hStream, attr, value)
910cdef CUresult cuEventCreate(CUevent* phEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
911 return _driver._cuEventCreate(phEvent, Flags) 2CbDb5 ? d e f g h i j k l m n o p q r s t u v w x 2cZe0e2e3e5e6e8e9e#e$e'e(egiNe-jnbHbOe.j6 ! H BbSj*q+q,qTj-q.q/q5m9N{c+ |c!N^n#NNmOmPmQmRmSmFbTmUmVmWmXm/jhi[c?jJ5'jmC9k!kqC(k)kgfhfhdidpbqbdheh/k:k~v)i*ibece{k-iVbrpxC.i|k}k/icw~kalblcldeyCeejhspdwdlel:i;iufvfwfxf=iyfzfAfBffegeglhliejendodmlnlrcscudvdWfXfrlslXsAhBhCCylzl4f5fydzdvbwbJhKhFlGlHCKlLlxeyeOlnjZb-pKCojPlQlpjkwRlSlTlUlzeLCAeOh5slwVlWlqjrj-f.f/f:fsj;f=f?f@fBeCeYlZlEeFeEdFd4l5lEcFcLdMdXhYh#l$l!s1h2hJeKeQC*l+lTC/l:lXC@l[l1C`l{l5Cambm9Cfmgm$Ckmlm(Cpmqm0mii,b
914cdef CUresult cuEventRecord(CUevent hEvent, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
915 return _driver._cuEventRecord(hEvent, hStream) 2CbDb5 ? d e f g h i j k l m n o p q r s t u v w x ! H BbSj*q+q,qTj-q.q/q5m{c+ |cNmOmPmQmRmSmFbTmUmVmWmXm/jhi[c?j'jJeKe0mii,b
918cdef CUresult cuEventRecordWithFlags(CUevent hEvent, CUstream hStream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
919 return _driver._cuEventRecordWithFlags(hEvent, hStream, flags)
922cdef CUresult cuEventQuery(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
923 return _driver._cuEventQuery(hEvent) 2giNeOeFb/jhi
926cdef CUresult cuEventSynchronize(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
927 return _driver._cuEventSynchronize(hEvent) 2+ Fbhi[c?j
930cdef CUresult cuEventDestroy(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
931 return _driver._cuEventDestroy_v2(hEvent) 2CbDb5 ? d e f g h i j k l m n o p q r s t u v w x zxAxBxCxDxExFxGxHxIxJxKxLxgiNe-jnbHbOe.j6 B ! H SjTj5m9N{c+ |c!N^n#NNmOmPmQmRmSmFbTmUmVmWmXm/jhi[c?jJ5'jiHMxNxCHOxPxQxRxptqt7x8x9x!x#x$xeI%x'x(x)x*x+x,x-xCI.x/x:x;x=x?x@x[xDI]xEI^x_xFI`x{x|x}x~xaybycydyeyfygyhyiyjykylymynyoypyqyrysytyuyvywyxyyyzyAyGyrtst#JSyTyUyVyttut#y$y%y'y(y)yNK*y+y,y-y.y/y:y;y#K=y?y@y[y]y^y_y`y$K{y%K|y}y'K~yazbzczdzezfzgzhzizjzkzlzmznzozpzqzrzsztzuzvzwzxzyzzzAzBzCzDzEzKzvtwtJeKejMWzXzBMYzZzTM0z1z#M2z3z]M4z5zkN6z7zCN8z9zUN!z#z0mii,b
934cdef CUresult cuEventElapsedTime(float* pMilliseconds, CUevent hStart, CUevent hEnd) except ?CUDA_ERROR_NOT_FOUND nogil:
935 return _driver._cuEventElapsedTime_v2(pMilliseconds, hStart, hEnd) 2{c+ |c[c
938cdef CUresult cuImportExternalMemory(CUexternalMemory* extMem_out, const CUDA_EXTERNAL_MEMORY_HANDLE_DESC* memHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
939 return _driver._cuImportExternalMemory(extMem_out, memHandleDesc)
942cdef CUresult cuExternalMemoryGetMappedBuffer(CUdeviceptr* devPtr, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_BUFFER_DESC* bufferDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
943 return _driver._cuExternalMemoryGetMappedBuffer(devPtr, extMem, bufferDesc)
946cdef CUresult cuExternalMemoryGetMappedMipmappedArray(CUmipmappedArray* mipmap, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC* mipmapDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
947 return _driver._cuExternalMemoryGetMappedMipmappedArray(mipmap, extMem, mipmapDesc)
950cdef CUresult cuDestroyExternalMemory(CUexternalMemory extMem) except ?CUDA_ERROR_NOT_FOUND nogil:
951 return _driver._cuDestroyExternalMemory(extMem)
954cdef CUresult cuImportExternalSemaphore(CUexternalSemaphore* extSem_out, const CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC* semHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
955 return _driver._cuImportExternalSemaphore(extSem_out, semHandleDesc)
958cdef CUresult cuSignalExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
959 return _driver._cuSignalExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream)
962cdef CUresult cuWaitExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
963 return _driver._cuWaitExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream)
966cdef CUresult cuDestroyExternalSemaphore(CUexternalSemaphore extSem) except ?CUDA_ERROR_NOT_FOUND nogil:
967 return _driver._cuDestroyExternalSemaphore(extSem)
970cdef CUresult cuStreamWaitValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
971 return _driver._cuStreamWaitValue32_v2(stream, addr, value, flags)
974cdef CUresult cuStreamWaitValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
975 return _driver._cuStreamWaitValue64_v2(stream, addr, value, flags)
978cdef CUresult cuStreamWriteValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
979 return _driver._cuStreamWriteValue32_v2(stream, addr, value, flags)
982cdef CUresult cuStreamWriteValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
983 return _driver._cuStreamWriteValue64_v2(stream, addr, value, flags)
986cdef CUresult cuStreamBatchMemOp(CUstream stream, unsigned int count, CUstreamBatchMemOpParams* paramArray, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
987 return _driver._cuStreamBatchMemOp_v2(stream, count, paramArray, flags)
990cdef CUresult cuFuncGetAttribute(int* pi, CUfunction_attribute attrib, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
991 return _driver._cuFuncGetAttribute(pi, attrib, hfunc)
994cdef CUresult cuFuncSetAttribute(CUfunction hfunc, CUfunction_attribute attrib, int value) except ?CUDA_ERROR_NOT_FOUND nogil:
995 return _driver._cuFuncSetAttribute(hfunc, attrib, value)
998cdef CUresult cuFuncSetCacheConfig(CUfunction hfunc, CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
999 return _driver._cuFuncSetCacheConfig(hfunc, config)
1002cdef CUresult cuFuncGetModule(CUmodule* hmod, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
1003 return _driver._cuFuncGetModule(hmod, hfunc)
1006cdef CUresult cuFuncGetName(const char** name, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
1007 return _driver._cuFuncGetName(name, hfunc) 2(8
1010cdef CUresult cuFuncGetParamInfo(CUfunction func, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil:
1011 return _driver._cuFuncGetParamInfo(func, paramIndex, paramOffset, paramSize)
1014cdef CUresult cuFuncIsLoaded(CUfunctionLoadingState* state, CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
1015 return _driver._cuFuncIsLoaded(state, function)
1018cdef CUresult cuFuncLoad(CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
1019 return _driver._cuFuncLoad(function)
1022cdef 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:
1023 return _driver._cuLaunchKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams, extra) 2PeQeWjXjYj%gZj0jReSe1j2j3j4j'g5j6j
1026cdef CUresult cuLaunchKernelEx(const CUlaunchConfig* config, CUfunction f, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil:
1027 return _driver._cuLaunchKernelEx(config, f, kernelParams, extra) 22 QcCbc C RdDb1bI 2b5 ?c? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S y ^ z A E kbF G Z 0 1 N ( )bWcXcXeYc! H Bb+ Fb[c*b# $ +bTe:j+h,h}c-h~c.h/had:h;h=h?h@h[h]h^h_hbd`h{h|h}h~haibicidieicdfi: lbmb
1030cdef 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:
1031 return _driver._cuLaunchCooperativeKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams)
1034cdef CUresult cuLaunchCooperativeKernelMultiDevice(CUDA_LAUNCH_PARAMS* launchParamsList, unsigned int numDevices, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1035 return _driver._cuLaunchCooperativeKernelMultiDevice(launchParamsList, numDevices, flags)
1038cdef CUresult cuLaunchHostFunc(CUstream hStream, CUhostFn fn, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil:
1039 return _driver._cuLaunchHostFunc(hStream, fn, userData) 2-b.b/b:b;b*
1042cdef CUresult cuFuncSetBlockShape(CUfunction hfunc, int x, int y, int z) except ?CUDA_ERROR_NOT_FOUND nogil:
1043 return _driver._cuFuncSetBlockShape(hfunc, x, y, z)
1046cdef CUresult cuFuncSetSharedSize(CUfunction hfunc, unsigned int bytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1047 return _driver._cuFuncSetSharedSize(hfunc, bytes)
1050cdef CUresult cuParamSetSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1051 return _driver._cuParamSetSize(hfunc, numbytes)
1054cdef CUresult cuParamSeti(CUfunction hfunc, int offset, unsigned int value) except ?CUDA_ERROR_NOT_FOUND nogil:
1055 return _driver._cuParamSeti(hfunc, offset, value)
1058cdef CUresult cuParamSetf(CUfunction hfunc, int offset, float value) except ?CUDA_ERROR_NOT_FOUND nogil:
1059 return _driver._cuParamSetf(hfunc, offset, value)
1062cdef CUresult cuParamSetv(CUfunction hfunc, int offset, void* ptr, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1063 return _driver._cuParamSetv(hfunc, offset, ptr, numbytes)
1066cdef CUresult cuLaunch(CUfunction f) except ?CUDA_ERROR_NOT_FOUND nogil:
1067 return _driver._cuLaunch(f)
1070cdef CUresult cuLaunchGrid(CUfunction f, int grid_width, int grid_height) except ?CUDA_ERROR_NOT_FOUND nogil:
1071 return _driver._cuLaunchGrid(f, grid_width, grid_height)
1074cdef CUresult cuLaunchGridAsync(CUfunction f, int grid_width, int grid_height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1075 return _driver._cuLaunchGridAsync(f, grid_width, grid_height, hStream)
1078cdef CUresult cuParamSetTexRef(CUfunction hfunc, int texunit, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1079 return _driver._cuParamSetTexRef(hfunc, texunit, hTexRef)
1082cdef CUresult cuFuncSetSharedMemConfig(CUfunction hfunc, CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
1083 return _driver._cuFuncSetSharedMemConfig(hfunc, config)
1086cdef CUresult cuGraphCreate(CUgraph* phGraph, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1087 return _driver._cuGraphCreate(phGraph, flags) 2bBcBdBeBfBgBhBiBjB%m^j'mkB_j(m)mlBmBnBoBpB[jqBrBsBtB' uBvBwBxByBzBx4ABBBCBDBEBFBGBHBIBJBKBLBMBNBOBPBQBRBSBTBUBVBWBXB*m+m`b`jZe0e{j,m-m.m/m)d1eoipiqiri:m;m=m?m{b|j2e3e}j@m[m]m^m*d4esitiuivi_m`m{m~j|mYBak}m~manbkbnckcndnenfn|bdk5e6eekgnhninjn+d7ewixiyiziknlnmnnn}bfk8e9egkonpnqnrn,d!eAiBiCiDisntnunvn~bhk#e$eikwnxnynzn-d%eEiFiGiHiAnBnCnDnacjk'e(ekkEnFnGnHn.d)eIiJiKiLiInJnKnlkLnmkMnNnOnnkPnokQnRn*eSnpkTnqkUnVn9mK5L5M5N5-zO5CAlutmatMe!mVd8b]c]q^q_q`q9b!b#b$bGb=b3c4c%b/ fu'dliYdZd0d1d2d3d4d5dgiNe-jnbHbOe.j3 T L 7g6 jbEb'b8g9gU V W !gX Y 7 8 #g$g9 ^c(b?b_c5c(j(dgu4 M D J K fO%r7m8mb #m7cB $m@b[b) 6cgO@jhuhOiujuDAEAkiIbFAiOP5?oicMs8k9k!k#knC@o[o]ocfdf6ioC_o`o|ojcOs'k(k)k*krC}o~oapefff7isCcpdpSbgfhf+k{g|g}g@dif8i~gahjf; kf[dhdid]d9i^d_d`dkclcjd!i{d|dpbqbTb| } ~ ab#irbchdhehfh$iepfpkd}dghQsgphpipmcRs.k/k:k;ktCjpkplpmfnf%iuCnpop=kUbpp(i)i*i+iaw?k@k[k~daehhbw^k_k`ksbbece,iofpfqfldrfihsftf{kVbrp.i|k}k/icw~kalbldeeejhdwdlel:i;iufvfwfxf=iyfzfAfBftbfegeCfDfEfhekhFfGftpncUsflglhlilupvpwpHfIf?izCxpyplhmhnhohzpApBpCpDp@iocphqhiejerhjlJfKfLfMfmdNfklOfPfpcndodpdke'c(cWb)c*c+cEpqcVsllmlnlolACFpGpHpQfRf[iBCJpKp, rcsc,cqdrdsdtdbbudvdleSfTfmeUfVfpltc]i^iWfXf_iLpshthuhYfnevhNpwhxhOpucqlrlsltlPpQpRpZf0f`iSpTp{iubulzhAhBhChYs|i}i~iwdxd1fZsbjcjUpVpvc0sxlylzlAlDCWpXpYp2f3fdjEC0p1pXb4f5fBlDhEhFhoe6fejGhHh7f= 8fpeydzdqefjresetewcxcAdhjuevevbwbYbcbdbebfbijxbIhJhKhLhjj2p3pBdweMh2s4p5p6pyc3sElFlGlHlFC7p8p9p!f#fkjGC#p$p%pzc4sJlKlLlMlIC'p(p)p$f%fljJC+p,pNlybxeyemj'f(f)fCd*fNh+f,fOlZb-pojPlQlpjkwRlSlTlzeAeOhlwVlWlqjrj-f.f/f:fsj;f=f?f@fzbBeCe[f]f^fDePh_f`f.pAc6sXlYlZl0l/p:p;p{f|ftjMC=p?pQhRhShTh@p[p]p^p_pujBcUhVhEeFeWh1l}f~fagbgDdcg2ldgegCcEdFdGdGe-c.c0b/c:c;c`pDc7s3l4l5l6lNC{p|p}pfgggvjOCaqbq- EcFc=cHdIdJdKdgbLdMdHehgigIejgkgcqGc7l8lXhYh9l8swjxjyjlgmgzj9sAjBjeqHc!l#l$l%lfqgqhqngogCjiqjqDjAb'l0h1h2h3h#sEjFjGjNdOdpg$sIjJjlqmqIc%s)l*l+l,lRCnqoqpqqgrgKjSCrqsqtqJc)s.l/l:l;lUCuqvqwqsgtgLjVCyqzqAqKc+s?l@l[l]lYCBqCqDqugvgMjZCFqGqHqLc-s_l`l{l|l2CIqJqKqwgxgNj3CMqNqOqMc/s~lambmcm6CPqQqRqygzgOj7CTqUqVqNc;semfmgmhm!CWqXqYqAgBgPj#C0q1q2qOc?sjmkmlmmm%C3q4q5qCgDgQj'C7q8q9qPc@sompmqmrm)C!q#q$qEgFgRj*C'q(q
1090cdef CUresult cuGraphAddKernelNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1091 return _driver._cuGraphAddKernelNode_v2(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2c C I ' 4b5b6bSc7bVjsm`b)d{b*d|b+d}b,d~b-dac.dMe9b!b#b$b%bT L 7g6 jbEb(b4 M D J K b ) iccfjcefSb@d; kcpbqbTb| } ~ abrbkdmcmfUb~dsbldVbdetbncHfocMfpcndodpdke'c(cWb)c*c+cqcQf, bbtcYfucZfubwdvc2fXboe= wcvbwbYbcbdbebfbxbBdyc!fzc$fybCdZbzezbAc{fBcbgCcEdFdGdGe-c.c0b/c:c;cDcfg- gbGclgHcngAbNdIcqgJcsgKcugLcwgMcygNcAgOcCgPcEg
1094cdef CUresult cuGraphKernelNodeGetParams(CUgraphNode hNode, CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1095 return _driver._cuGraphKernelNodeGetParams_v2(hNode, nodeParams) 2c 1bI 2bjO9b!b#b$b%b(bb
1098cdef CUresult cuGraphKernelNodeSetParams(CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1099 return _driver._cuGraphKernelNodeSetParams_v2(hNode, nodeParams)
1102cdef CUresult cuGraphAddMemcpyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1103 return _driver._cuGraphAddMemcpyNode(phGraphNode, hGraph, dependencies, numDependencies, copyParams, ctx) 2@ [ ] ib1e4e7e!e%e)e8b/ 3 'bU V W X Y dfffiflc}dnfaerfeeheIfmdWbRf, rcsc,cqdrdsdtdmene0fxd3f6fxcwe#f%f*fAeDe|fDd0bgg- EcFc=cHdIdJdKdIemgogOdrgtgvgxgzgBgDgFg
1106cdef CUresult cuGraphMemcpyNodeGetParams(CUgraphNode hNode, CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1107 return _driver._cuGraphMemcpyNodeGetParams(hNode, nodeParams) 2Ib
1110cdef CUresult cuGraphMemcpyNodeSetParams(CUgraphNode hNode, const CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1111 return _driver._cuGraphMemcpyNodeSetParams(hNode, nodeParams)
1114cdef 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:
1115 return _driver._cuGraphAddMemsetNode(phGraphNode, hGraph, dependencies, numDependencies, memsetParams, ctx) 2@ [ ] ibTcUcVc@coipiqirisitiuiviwixiyiziAiBiCiDiEiFiGiHiIiJiKiLi7 8 9 b 7c6i7i8ijdgh%ihhihjhkh?iNf)c[ibbudvdleSfTfmeUfVfvh`i1fdjejAdMhkjljNhOhPhtjcg/cvjgbLdMdHehgigIejgkgzjCjpgKjLjMjNjOjPjQjRj
1118cdef CUresult cuGraphMemsetNodeGetParams(CUgraphNode hNode, CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1119 return _driver._cuGraphMemsetNodeGetParams(hNode, nodeParams) 1b
1122cdef CUresult cuGraphMemsetNodeSetParams(CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1123 return _driver._cuGraphMemsetNodeSetParams(hNode, nodeParams)
1126cdef CUresult cuGraphAddHostNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1127 return _driver._cuGraphAddHostNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 27d8d9d,m-m@m[mgnhnonpnwnxnEnFn]cGb=b3c4c'dliYdZd0d1d2d3d4d5d3 ^c?b_c5c(dguB @b[b6c@o}o{g^dTb$ijp?kof~k;i=iCfuplhmhnhohJfkeFp,cleshPp|iWpDhreYbjj7p'p'fRlrjsj[f/pQhRhShTh}fGe{p=cHewjfqEjnquqBqIqPqWq3q!q
1130cdef CUresult cuGraphHostNodeGetParams(CUgraphNode hNode, CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1131 return _driver._cuGraphHostNodeGetParams(hNode, nodeParams) 2* 'd^c_c(d
1134cdef CUresult cuGraphHostNodeSetParams(CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1135 return _driver._cuGraphHostNodeSetParams(hNode, nodeParams)
1138cdef CUresult cuGraphAddChildGraphNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1139 return _driver._cuGraphAddChildGraphNode(phGraphNode, hGraph, dependencies, numDependencies, childGraph) 22 ' `b{b|b}b~bac* %bfu'dli^c(b_c(dicjcSb; pbqbTb| } ~ abrbmcUbsbVbtbncocpcqc, bbtcucubvcXb= vbwbYbcbdbebfbxbyczcybZbzbAcBcCcDc- gbGcHcAbIcJcKcLcMcNcOcPc
1142cdef CUresult cuGraphChildGraphNodeGetGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1143 return _driver._cuGraphChildGraphNodeGetGraph(hNode, phGraph) 22 ' `b{b|b}b~bac* %bfu'dli^c(b_c(dicjcSb; pbqbTb| } ~ abrbmcUbsbVbtbncocpcqc, bbtcucubvcXb= vbwbYbcbdbebfbxbyczcybZbzbAcBcCcDc- gbGcHcAbIcJcKcLcMcNcOcPc
1146cdef CUresult cuGraphAddEmptyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1147 return _driver._cuGraphAddEmptyNode(phGraphNode, hGraph, dependencies, numDependencies) 2^j_j[j@ [ ] ib|s}s~s`j1e|j4e~jakbkckdk7efk!ehk%ejk)elkmknkok*epkqkCAtm4 M D J K fO%r7m8m#m$m@b[b@jhuiujuDAEAFAiO8kdf'kffif[dlcch}d.knf(iae`ksbbece,iofpfqfldrfihsftf.ieeheflIfqhmdWbllRf, rcsc,cqdrdsdtdme^ineql0fzhxdxl3f6fpexcIhweEl#fJl%fNlybxeyemj'f(f)fCd*fNh+f,fojAeDeXl|fVhDd0b3lgg- EcFc=cHdIdJdKdIe8lmg!log0hOd)lrg.ltg?lvg_lxg~lzgemBgjmDgomFg
1150cdef CUresult cuGraphAddEventRecordNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1151 return _driver._cuGraphAddEventRecordNode(phGraphNode, hGraph, dependencies, numDependencies, event) 22cZe2e5e8e#e'egiNe-jnbHb6 9k(kgfhdpbdh/k)ibe|k:i;iufvfwfxffegliendmlrcudWfrlAhyl4fydvbJhFlKlxePlqjrj-f.f/f:fBeYlEeEd4lEcLdXh#l1h*l/l@l`lamfmkmpm
1154cdef CUresult cuGraphEventRecordNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1155 return _driver._cuGraphEventRecordNodeGetEvent(hNode, event_out)
1158cdef CUresult cuGraphEventRecordNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1159 return _driver._cuGraphEventRecordNodeSetEvent(hNode, event)
1162cdef CUresult cuGraphAddEventWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1163 return _driver._cuGraphAddEventWaitNode(phGraphNode, hGraph, dependencies, numDependencies, event) 22c0e3e6e9e$e(enbHbOe.j!k)khfidqbeh:k*ice}k:i=iyfzfAfBfgehljeodnlscvdXfslBhzl5fzdwbKhGlLlyeQlqjsj;f=f?f@fCeZlFeFd5lFcMdYh$l2h+l:l[l{lbmgmlmqm
1166cdef CUresult cuGraphEventWaitNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1167 return _driver._cuGraphEventWaitNodeGetEvent(hNode, event_out)
1170cdef CUresult cuGraphEventWaitNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1171 return _driver._cuGraphEventWaitNodeSetEvent(hNode, event)
1174cdef 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:
1175 return _driver._cuGraphAddExternalSemaphoresSignalNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
1178cdef CUresult cuGraphExternalSemaphoresSignalNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1179 return _driver._cuGraphExternalSemaphoresSignalNodeGetParams(hNode, params_out)
1182cdef CUresult cuGraphExternalSemaphoresSignalNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1183 return _driver._cuGraphExternalSemaphoresSignalNodeSetParams(hNode, nodeParams)
1186cdef 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:
1187 return _driver._cuGraphAddExternalSemaphoresWaitNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
1190cdef CUresult cuGraphExternalSemaphoresWaitNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_WAIT_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1191 return _driver._cuGraphExternalSemaphoresWaitNodeGetParams(hNode, params_out)
1194cdef CUresult cuGraphExternalSemaphoresWaitNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1195 return _driver._cuGraphExternalSemaphoresWaitNodeSetParams(hNode, nodeParams)
1198cdef 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:
1199 return _driver._cuGraphAddBatchMemOpNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
1202cdef CUresult cuGraphBatchMemOpNodeGetParams(CUgraphNode hNode, CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1203 return _driver._cuGraphBatchMemOpNodeGetParams(hNode, nodeParams_out)
1206cdef CUresult cuGraphBatchMemOpNodeSetParams(CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1207 return _driver._cuGraphBatchMemOpNodeSetParams(hNode, nodeParams)
1210cdef CUresult cuGraphExecBatchMemOpNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1211 return _driver._cuGraphExecBatchMemOpNodeSetParams(hGraphExec, hNode, nodeParams)
1214cdef CUresult cuGraphAddMemAllocNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUDA_MEM_ALLOC_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1215 return _driver._cuGraphAddMemAllocNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2-C.C]skubx/Ccx%m^j'm_j(m)m^sSdTdUdLe@ [ ] ibTcUcVc@c_s`s{s|s}s~s*m+m`jZe0e{j)d1eoipiqiri=m?m|j2e3e}j*d4esitiuivi{m~j|mak}m~manbkbnckcndnenfndk5e6eek+d7ewixiyizimnnnfk8e9egk,d!eAiBiCiDiunvnhk#e$eik-d%eEiFiGiHiCnDnjk'e(ekk.d)eIiJiKiLiKnlkLnmkMnNnOnnkPnokQnRnSnpkTnqkUnVntmatVdNeOeB ki?o8k#kdf6i|o'k*kff7iSbgfhf+k{g|g}g@dif8i~gahjf[d]dlcjd#ichfh}dghip.k;knf%i=k(i+iaehh`ksbbece,iofpfqfldrfihsftf{k.i/ieejhtbfegeCfDfEfhekhFfGftpflilIf?i@iqhrhmdNfpdWb)cEpllolRf[i, rcsc,cqdrdsdtdbbudvdleSfTfmeUfVfpl^i_inevhOpqltl0f`i{izhChxd1fVpxlAl3fdjXb4f5fBlDhEhFhoe6fejGhHh7fpeqexcAdijIhLhweMh6pElHl#fkj%pJlMl%fljNlybxeyemj'f(f)fCd*fNh+f,fOlojpjAeOhzbBeCe[f]f^fDePh_f`f.pXl0l|ftjujVhWhDdcgGd0b/c`p3l6lggvj- EcFc=cHdIdJdKdgbLdMdHehgigIejgkgcq8l9lmgzjeq!l%logCjDj0h3hOdpgmq)l,lrgKjtq.l;ltgLjAq?l]lvgMjHq_l|lxgNjOq~lcmzgOjVqemhmBgPj2qjmmmDgQj9qomrmFgRj
1218cdef CUresult cuGraphMemAllocNodeGetParams(CUgraphNode hNode, CUDA_MEM_ALLOC_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1219 return _driver._cuGraphMemAllocNodeGetParams(hNode, params_out) 2kOlOmOnOoOpOqOrOsOtOuOvOwOxOyOzOAOBOCODOEOFOGOGAHAIAJAKALAMANAOAPAQA
1222cdef CUresult cuGraphAddMemFreeNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
1223 return _driver._cuGraphAddMemFreeNode(phGraphNode, hGraph, dependencies, numDependencies, dptr) 2]s^sSdTdUdLe@ [ ] ibTcUcVc@c{j}jekgkikkkluki#k*k+k]dfh;k+i,i/itbfegeCfDfEfhekhFfGfilrhpdol_itlChAlBlqeLhHlMlmjpjzbBeCe[f]f^fDePh_f`f0lWhGd6l9l%l3h,l;l]l|lcmhmmmrm
1226cdef CUresult cuGraphMemFreeNodeGetParams(CUgraphNode hNode, CUdeviceptr* dptr_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1227 return _driver._cuGraphMemFreeNodeGetParams(hNode, dptr_out)
1230cdef CUresult cuDeviceGraphMemTrim(CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
1231 return _driver._cuDeviceGraphMemTrim(device) 1_`{
1234cdef CUresult cuDeviceGetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1235 return _driver._cuDeviceGetGraphMemAttribute(device, attr, value) 2_ ` { )8ki
1238cdef CUresult cuDeviceSetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1239 return _driver._cuDeviceSetGraphMemAttribute(device, attr, value) 1_`{
1242cdef CUresult cuGraphClone(CUgraph* phGraphClone, CUgraph originalGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1243 return _driver._cuGraphClone(phGraphClone, originalGraph) 2GbnbL jbW
1246cdef CUresult cuGraphNodeFindInClone(CUgraphNode* phNode, CUgraphNode hOriginalNode, CUgraph hClonedGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1247 return _driver._cuGraphNodeFindInClone(phNode, hOriginalNode, hClonedGraph) 2' `b{b|b}b~bac* %b'dli^c(b_cicjcSb; pbqbTb| } ~ abrbmcUbsbVbtbncocpcqc, bbtcucubvcXb= vbwbYbcbdbebfbxbyczcybZbzbAcBcCcDc- gbGcHcAbIcJcKcLcMcNcOcPc
1250cdef CUresult cuGraphNodeGetType(CUgraphNode hNode, CUgraphNodeType* type) except ?CUDA_ERROR_NOT_FOUND nogil:
1251 return _driver._cuGraphNodeGetType(hNode, type) 2c 1bI 2bjOkOlOmOnOoOpOqOrOsOtOuOvOwOxOyOzOAOBOCODOEOFOGOGAHAIAJAKALAMAHONAOAPAQA*8+8,8-8.8/8:8;8=8?8@8[8]8^8_8`8{8|8}89b!b#b$b* %b'dYdZd0d1d2d3d4d5d^c(b_c(j(db
1254cdef CUresult cuGraphGetNodes(CUgraph hGraph, CUgraphNode* nodes, size_t* numNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1255 return _driver._cuGraphGetNodes(hGraph, nodes, numNodes) 2c C 1bI 2b,z[jjOkOlO~8mOnOoOa9b9c9pOqOrOsOtOuOd9e9f9g9h9i9j9k9l9vOwOm9xOyOzOAOn9o9p9q9BOCODOEOFOGOr9s9t9u9v9w9x9y9CA]q^q_q`q9b!b#b$b* %b'dYdZd0d1d2d3d4d5d^c(b_c(j(d4 M D J K b 7cB
1258cdef CUresult cuGraphGetRootNodes(CUgraph hGraph, CUgraphNode* rootNodes, size_t* numRootNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1259 return _driver._cuGraphGetRootNodes(hGraph, rootNodes, numRootNodes)
1262cdef CUresult cuGraphGetEdges(CUgraph hGraph, CUgraphNode* from_, CUgraphNode* to, CUgraphEdgeData* edgeData, size_t* numEdges) except ?CUDA_ERROR_NOT_FOUND nogil:
1263 return _driver._cuGraphGetEdges_v2(hGraph, from_, to, edgeData, numEdges) 2z9A9B9C9D9E9F9[j4 M D J K b 7cB hu
1266cdef CUresult cuGraphNodeGetDependencies(CUgraphNode hNode, CUgraphNode* dependencies, CUgraphEdgeData* edgeData, size_t* numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1267 return _driver._cuGraphNodeGetDependencies_v2(hNode, dependencies, edgeData, numDependencies) 2]s^s[j|s}s~sVjGAHAG9IAJAKALAH9I9J9K9MAHONAOAPAQAL9M9N9O9P9Q9R9S9tm6 J 7m8mb huju
1270cdef CUresult cuGraphNodeGetDependentNodes(CUgraphNode hNode, CUgraphNode* dependentNodes, CUgraphEdgeData* edgeData, size_t* numDependentNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1271 return _driver._cuGraphNodeGetDependentNodes_v2(hNode, dependentNodes, edgeData, numDependentNodes) 2[jGAHAIAJAKALAMAHONAOAPAQAT9U9V9W9X9Y9D K %r7m8mb #m$mju
1274cdef CUresult cuGraphAddDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1275 return _driver._cuGraphAddDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 2[jD J K %r7m8mb #m7c$m
1278cdef CUresult cuGraphRemoveDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1279 return _driver._cuGraphRemoveDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 2K %r7m8mb
1282cdef CUresult cuGraphDestroyNode(CUgraphNode hNode) except ?CUDA_ERROR_NOT_FOUND nogil:
1283 return _driver._cuGraphDestroyNode(hNode) 2*e* Gb=b/ fu'dliYdZd0d1d2d3d4d5d^c?b_c(dM D J 7cB iO
1286cdef CUresult cuGraphInstantiate(CUgraphExec* phGraphExec, CUgraph hGraph, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1287 return _driver._cuGraphInstantiateWithFlags(phGraphExec, hGraph, flags) 2GbnbL jbW @jkiIbFA
1290cdef CUresult cuGraphInstantiateWithParams(CUgraphExec* phGraphExec, CUgraph hGraph, CUDA_GRAPH_INSTANTIATE_PARAMS* instantiateParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1291 return _driver._cuGraphInstantiateWithParams(phGraphExec, hGraph, instantiateParams) 2-b.b/b:b;b)g2 Qcc C I 5 ? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S 7dSdTdUdLe' 2c8d9d4b5b6bSc7b@ [ ] ibTcUcVc@cQ5R5S5_s`s{sMeVd]c=b3c4c/ Hb3 T 6 EbU V X Y 7 8 9 ?b5c4 M D J K b B Zc0c1c!d#d$dy z A E F G Z 0 1 ]b^b_b_ ` { @b[bN ( ) 6c)bWcXcYc%
1294cdef CUresult cuGraphExecGetFlags(CUgraphExec hGraphExec, cuuint64_t* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1295 return _driver._cuGraphExecGetFlags(hGraphExec, flags)
1298cdef CUresult cuGraphExecKernelNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1299 return _driver._cuGraphExecKernelNodeSetParams_v2(hGraphExec, hNode, nodeParams)
1302cdef CUresult cuGraphExecMemcpyNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1303 return _driver._cuGraphExecMemcpyNodeSetParams(hGraphExec, hNode, copyParams, ctx)
1306cdef CUresult cuGraphExecMemsetNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1307 return _driver._cuGraphExecMemsetNodeSetParams(hGraphExec, hNode, memsetParams, ctx)
1310cdef CUresult cuGraphExecHostNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1311 return _driver._cuGraphExecHostNodeSetParams(hGraphExec, hNode, nodeParams)
1314cdef CUresult cuGraphExecChildGraphNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1315 return _driver._cuGraphExecChildGraphNodeSetParams(hGraphExec, hNode, childGraph)
1318cdef CUresult cuGraphExecEventRecordNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1319 return _driver._cuGraphExecEventRecordNodeSetEvent(hGraphExec, hNode, event)
1322cdef CUresult cuGraphExecEventWaitNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1323 return _driver._cuGraphExecEventWaitNodeSetEvent(hGraphExec, hNode, event)
1326cdef CUresult cuGraphExecExternalSemaphoresSignalNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1327 return _driver._cuGraphExecExternalSemaphoresSignalNodeSetParams(hGraphExec, hNode, nodeParams)
1330cdef CUresult cuGraphExecExternalSemaphoresWaitNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1331 return _driver._cuGraphExecExternalSemaphoresWaitNodeSetParams(hGraphExec, hNode, nodeParams)
1334cdef CUresult cuGraphNodeSetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1335 return _driver._cuGraphNodeSetEnabled(hGraphExec, hNode, isEnabled)
1338cdef CUresult cuGraphNodeGetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int* isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1339 return _driver._cuGraphNodeGetEnabled(hGraphExec, hNode, isEnabled)
1342cdef CUresult cuGraphUpload(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1343 return _driver._cuGraphUpload(hGraphExec, hStream) 25 hb7dSdTdUd' 2c8d9d4b5b6b7b@ [ ] TcUcVc3c4c5cy z A E F G Z 0 1 ]b^b_b_ ` {
1346cdef CUresult cuGraphLaunch(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1347 return _driver._cuGraphLaunch(hGraphExec, hStream) 2-b.b/b:b;b2 c C I 5 . hbd e f g h i j k l m n o p q r s O t u v w x P Q R S 7dSdTdUdLe' 2c8d9d4b5b6bSc7b@ [ ] ibTcUcVc@cVd]cGb=b3c4cnbHb3 T L 6 jbEbU V W X Y 7 8 9 ?b5c4 M D J K b B y z A E F G Z 0 1 ]b^b_b_ ` { @b[bN ( ) 6ckiIb%
1350cdef CUresult cuGraphExecDestroy(CUgraphExec hGraphExec) except ?CUDA_ERROR_NOT_FOUND nogil:
1351 return _driver._cuGraphExecDestroy(hGraphExec) 2-b.b/b:b;b)g2 Qcc C I 5 ? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S 7dSdTdUdLe' 2c8d9d4b5b6bSc7b@ [ ] ibTcUcVc@cQ5R5S5_s`s{sMeVd]cGb=b3c4c/ nbHb3 T L 6 jbEbU V W X Y 7 8 9 ?b5c4 M D J K b B Zc0c1c!d#d$dy z A E F G Z 0 1 ]b^b_b_ ` { @b[bN ( ) 6c)bWcXcYc@jIbFA%
1354cdef CUresult cuGraphDestroy(CUgraph hGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1355 return _driver._cuGraphDestroy(hGraph) 2-b)j.b/b:b;b)g2 QcCbc 6dC Rd*jDb1bI 2b+j5 ?c,j? . hb3bRcd e f g h i j k l m n o p q r s O t u v w x P Q R S 'E(E)E*E+E,E-E.E/E:E;E=E?E@E[E]E^E_E`E{E|E[j}E~EaFbF' cFzxdFeFfFgFhFiFjFkFlFmFnFoFpFqFrFsFtFuFvFwFxFyFzFAFBFCFDFEFFF`bGFAxBxHFIFJFKFLFMFNFOFPFQFRFSFTFUF{bVFCxDxWFXFYFZF0F1F2F3F4F5F6F7F8F9F!F#F$F%F'F(F)F*F+F,F-F.F/F|b:F;FExFx=F?F@F[F]F^F_F`F{F|F}F~FaGbGcG}bdGeGGxHxfGgGhGiGjGkGlGmGnGoGpGqGrGsGtG~buGvGIxJxwGxGyGzGAGBGCGDGEGFGGGHGIGJGKGacLGMGKxLxNGOGPGQGRGSGTGUGVGWGXGYGZG0G1G2G3G4G5G6G7G8G9G!G#G*e$G%G'G(G)G*G9mK5L5M5N5-zO5CAlutmatMe!mVd8b]c]q^q_q`q9b!b#b$b* Gb=b3c4c%b/ fu'dliYdZd0d1d2d3d4d5dgiNe-jnbHbOe.j3 T L 7g6 jbEb'b8g9gU V W !gX Y 7 8 #g$g9 ^c(b?b_c5c(j(dgu4 M D J K fO%r7m8mb #m7cB $mZc0c1c!d#d$dy z A E F G Z 0 1 ]b^b_b_ ` { @b[bN ( ) 6c)bWcXcXeYc! @jhuhOiujuDAEAkiIbP5dHicfHgHhHMxNxjHkHlHmHnHoHpHqHrHtHuHxHjczHAHBHOxPxDHEHFHGHHHIHJHKHLHNHOHSbPHQxRxQHRHSHTHUHVHWHXHYHSx; TxUxVxptqtWxXxYxZx0x1x2x3x4x5x6xpb7xqb8xTb2H| 3H} 4H~ 5Hab6H7Hrb8H9H9x!x!H#H$H%H'H(H)H*H+H,H-Hmc/H:H;H#x$x=H?H@H[H]H^H_H`H{H|H}H~HUbbIcIdI%x'xfIgIhIiIjIkIlImInIpIqIrIsbsI(x)xtIuIvIwIxIyIzIAIBI*xVb,x-x.x/x:x;x=x?x@x[x]x^x_x`x{x|x}x~xaybycydyeyfygyhyiytbGIjykyHIIIJIKILIMINIOIncPIQIRIlymySITIUIVIWIXIYIZI0I1I2I3I4I5I6I7I8I9I!I#Ioc$I%I'Inyoy(I)I*I+I,I-I.I/I:I;I=Ipc?Ipyqy@I[I]I^I_I`I{I|I}Iqc~IaJbJrysycJdJeJfJgJhJiJjJkJlJmJ, nJtyuyoJpJqJrJsJbbtJvywyuJvJwJxJyJzJAJtcBJCJDJxyyyEJFJGJHJIJJJKJLJMJNJOJPJucQJRJzyAySJTJUJVJWJXJYJZJ0JByubDyEyFyrtstHyIyJyKyLyMyNyOyPyQyRy5J6Jvc8J9J!JSyTy$J%J'J(J)J*J+J,J-J/J:JXb;JUyVy=J?J@J[J]J^J_J`J{JWy= XyYyZyttut0y1y2y3y4y5y6y7y8y9y!yvb#ywb$yYbaKcbbKdbcKebdKfbeKfKxbgKhK%y'yiKjKkKlKmKnKoKpKqKrKsKycuKvKwK(y)yxKyKzKAKBKCKDKEKFKGKHKIKzcKKLKMK*y+yOKPKQKRKSKTKUKVKWKYKZK0Kyb1K,y-y2K3K4K5K6K7K8K9K!K.yZb:y;y=y?y@y[y]y^y_y`y{y|y}y~yazbzczdzezfzgzhzizjzkzlzmzzb(Knzoz)K*K+K,K-K.K/K:KAc;K=K?Kpzqz@K[K]K^K_K`K{K|K}K~KaLbLcLdLeLfLgLhLiLjLBckLlLmLrzsznLoLpLqLrLsLtLuLvLwLxLCcyLtzuzzLALBLCLDLELFLGLHLDcILJLKLvzwzLLMLNLOLPLQLRLSLTLULVL- WLxzyzXLYLZL0L1Lgb2LzzAz3L4L5L6L7L8L9LGc!L#L$LBzCz%L'L(L)L*L+L,L-L.L/L:L;LHc=L?LDzEz@L[L]L^L_L`L{L|L}LFzAbHzIzJzvtwtLzMzNzOzPzQzRzSzTzUzVzdMeMIcgMhMiMWzXzkMlMmMnMoMpMqMrMsMuMvMwMJcyMzMAMYzZzCMDMEMFMGMHMIMJMKMMMNMOMKcQMRMSM0z1zUMVMWMXMYMZM0M1M2M4M5M6MLc8M9M!M2z3z$M%M'M(M)M*M+M,M-M/M:M;MMc?M@M[M4z5z^M_M`M{M|M}M~MaNbNdNeNfNNchNiNjN6z7zlNmNnNoNpNqNrNsNtNvNwNxNOczNANBN8z9zDNENFNGNHNINJNKNLNNNONPNPcRNSNTN!z#zVNWNXNYNZN0N1N2N3N5N6N%
1358cdef CUresult cuGraphExecUpdate(CUgraphExec hGraphExec, CUgraph hGraph, CUgraphExecUpdateResultInfo* resultInfo) except ?CUDA_ERROR_NOT_FOUND nogil:
1359 return _driver._cuGraphExecUpdate_v2(hGraphExec, hGraph, resultInfo) 2@b[bN ( ) 6c)b
1362cdef CUresult cuGraphKernelNodeCopyAttributes(CUgraphNode dst, CUgraphNode src) except ?CUDA_ERROR_NOT_FOUND nogil:
1363 return _driver._cuGraphKernelNodeCopyAttributes(dst, src)
1366cdef CUresult cuGraphKernelNodeGetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, CUkernelNodeAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1367 return _driver._cuGraphKernelNodeGetAttribute(hNode, attr, value_out)
1370cdef CUresult cuGraphKernelNodeSetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, const CUkernelNodeAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1371 return _driver._cuGraphKernelNodeSetAttribute(hNode, attr, value)
1374cdef CUresult cuGraphDebugDotPrint(CUgraph hGraph, const char* path, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1375 return _driver._cuGraphDebugDotPrint(hGraph, path, flags) 2bxcx!
1378cdef CUresult cuUserObjectCreate(CUuserObject* object_out, void* ptr, CUhostFn destroy, unsigned int initialRefcount, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1379 return _driver._cuUserObjectCreate(object_out, ptr, destroy, initialRefcount, flags) 2-b.b/b:b;bc C I 7d' 2c8d9d4b5b6bSc7bVjsm`bZe0e,m-m)d{b2e3e@m[m*d|b5e6egnhn+d}b8e9eonpn,d~b#e$ewnxn-dac'e(eEnFn.dMe8b]c9b!b#b$b* Gb=b3c4c%b/ 'dliYdZd0d1d2d3d4d5dgiNe-jnbHbOe.j3 T L 7g6 jbEb'bU V W X Y 7 8 9 ^c(b?b_c5c(dgu4 M D J K b B @b[b) 6cic9k!k@ocfjc(k)k}oefSbgfhf{g@d; hdid^dkcpbqbTb| } ~ abrbdheh$ikdmc/k:kjpmfUb)i*i?k~dsbbeceofldVb|k}k~kde:i;iufvfwfxf=iyfzfAfBftbfegeCfncglhlupHflhmhnhohociejeJfMfpcndodpdke'c(cWb)c*c+cqcmlnlFpQf, rcsc,cbbudvdletcWfXfshYfucrlslPpZfubAhBh|iwdvcylzlWp2fXb4f5fDhoe= ydzdrewcvbwbYbcbdbebfbxbJhKhjjBdycFlGl7p!fzcKlLl'p$fybxeye'fCdZbPlQlRlzeqjrj-f.f/f:fsj;f=f?f@fzbBeCe[fAcYlZl/p{fQhRhShThBcEeFe}fbgCcEdFdGdGe-c.c0b/c:c;cDc4l5l{pfg- EcFc=cgbLdMdHeGcXhYhwjlgHc#l$lfqngAb1h2hEjNdIc*l+lnqqgJc/l:luqsgKc@l[lBqugLc`l{lIqwgMcambmPqygNcfmgmWqAgOckmlm3qCgPcpmqm!qEg
1382cdef CUresult cuUserObjectRetain(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1383 return _driver._cuUserObjectRetain(object, count)
1386cdef CUresult cuUserObjectRelease(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1387 return _driver._cuUserObjectRelease(object, count)
1390cdef CUresult cuGraphRetainUserObject(CUgraph graph, CUuserObject object, unsigned int count, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1391 return _driver._cuGraphRetainUserObject(graph, object, count, flags) 2-b.b/b:b;bc C I 7d' 2c8d9d4b5b6bSc7bVjsm`bZe0e,m-m)d{b2e3e@m[m*d|b5e6egnhn+d}b8e9eonpn,d~b#e$ewnxn-dac'e(eEnFn.dMe8b]c9b!b#b$b* Gb=b3c4c%b/ 'dliYdZd0d1d2d3d4d5dgiNe-jnbHbOe.j3 T L 7g6 jbEb'bU V W X Y 7 8 9 ^c(b?b_c5c(dgu4 M D J K b B @b[b) 6cic9k!k@ocfjc(k)k}oefSbgfhf{g@d; hdid^dkcpbqbTb| } ~ abrbdheh$ikdmc/k:kjpmfUb)i*i?k~dsbbeceofldVb|k}k~kde:i;iufvfwfxf=iyfzfAfBftbfegeCfncglhlupHflhmhnhohociejeJfMfpcndodpdke'c(cWb)c*c+cqcmlnlFpQf, rcsc,cbbudvdletcWfXfshYfucrlslPpZfubAhBh|iwdvcylzlWp2fXb4f5fDhoe= ydzdrewcvbwbYbcbdbebfbxbJhKhjjBdycFlGl7p!fzcKlLl'p$fybxeye'fCdZbPlQlRlzeqjrj-f.f/f:fsj;f=f?f@fzbBeCe[fAcYlZl/p{fQhRhShThBcEeFe}fbgCcEdFdGdGe-c.c0b/c:c;cDc4l5l{pfg- EcFc=cgbLdMdHeGcXhYhwjlgHc#l$lfqngAb1h2hEjNdIc*l+lnqqgJc/l:luqsgKc@l[lBqugLc`l{lIqwgMcambmPqygNcfmgmWqAgOckmlm3qCgPcpmqm!qEg
1394cdef CUresult cuGraphReleaseUserObject(CUgraph graph, CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1395 return _driver._cuGraphReleaseUserObject(graph, object, count) 2* Gb=b/ ^c?b_c(dM D
1398cdef CUresult cuGraphAddNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1399 return _driver._cuGraphAddNode_v2(phGraphNode, hGraph, dependencies, dependencyData, numDependencies, nodeParams) 2c 6dC d e f g h i j k l m n o p q r s O t u v w x P Q R S ,z.m/m:m;m]m^m_m`minjnknlnqnrnsntnynznAnBnGnHnInJn9m!m]q^q_q`q9b!b#b$bYdZd0d1d2d3d4d5d(jN ! gOiuIb[o]o_o`o~oapcpdp|g}g~gah_d`d{d|d| } ~ abepfpgphpkplpnpop@k[k^k_kpfqfsftfalbldlelufvfwfxfyfzfAfBfDfEfFfGfvpwpxpyplhmhnhohzpApBpCpDpKfLfOfPf'c(c*c+cGpHpJpKpqdrdsdtdSfTfUfVfthuhwhxhQpRpSpTp}i~ibjcjUpXpYp0p1pEhFhGhHhseteuevecbdbebfb2p3p4p5p8p9p#p$p(p)p+p,p(f)f+f,fSlTlVlWl-f.f/f:f;f=f?f@f]f^f_f`f:p;p=p?pQhRhShTh@p[p]p^p_p~fagdgeg-c.c:c;c|p}paqbqHdIdJdKdhgigjgkgxjyjAjBjgqhqiqjqFjGjIjJjlqoqpqrqsqvqwqyqzqCqDqFqGqJqKqMqNqQqRqTqUqXqYq0q1q4q5q7q8q#q$q'q(q
1402cdef CUresult cuGraphNodeSetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1403 return _driver._cuGraphNodeSetParams(hNode, nodeParams) 2Ib
1406cdef CUresult cuGraphExecNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1407 return _driver._cuGraphExecNodeSetParams(hGraphExec, hNode, nodeParams) 2Ib
1410cdef CUresult cuGraphConditionalHandleCreate(CUgraphConditionalHandle* pHandle_out, CUgraph hGraph, CUcontext ctx, unsigned int defaultLaunchValue, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1411 return _driver._cuGraphConditionalHandleCreate(pHandle_out, hGraph, ctx, defaultLaunchValue, flags) 2c 6dC d e f g h i j k l m n o p q r s O t u v w x P Q R S ,z.m/m:m;m]m^m_m`minjnknlnqnrnsntnynznAnBnGnHnInJn9m-z!m]q^q_q`q9b!b#b$bYdZd0d1d2d3d4d5d(jN ! gOMs[o]o_o`oOs~oapcpdp|g}g~gahkf_d`d{d|d| } ~ ab#irbchdhehfh$iepfpkd}dghQsgphpRskplpnpoppp@k[k^k_kpfqfsftfrpalbldlelufvfwfxfyfzfAfBfDfEfFfGfUsvpwpxpyplhmhnhohzpApBpCpDpphKfLfOfPf'c(c*c+cVsGpHpJpKpqdrdsdtdSfTfUfVf]ithuhwhxhQpRpSpTpul}i~ibjcjUp0sXpYp0p1pEhFhGhHh8fseteuevecbdbebfbijxbIhJhKhLhjj2p3pBdweMh2s4p5p3s8p9p#p$p4s(p)p+p,p(f)f+f,f-pSlTlVlWl-f.f/f:f;f=f?f@f]f^f_f`f6s:p;p=p?pQhRhShTh@p[p]p^p_pUh~fagdgeg-c.c:c;c7s|p}paqbqHdIdJdKdhgigjgkg7lxjyjAjBjgqhqiqjq'lFjGjIjJjlq%soqpqrqsq)svqwqyqzq+sCqDqFqGq-sJqKqMqNq/sQqRqTqUq;sXqYq0q1q?s4q5q7q8q@s#q$q'q(q
1414cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize) except ?CUDA_ERROR_NOT_FOUND nogil:
1415 return _driver._cuOccupancyMaxActiveBlocksPerMultiprocessor(numBlocks, func, blockSize, dynamicSMemSize) 2Tegxhxixjxkxlxmxnxoxpxqxrxsxtxuxvxwxxx
1418cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1419 return _driver._cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(numBlocks, func, blockSize, dynamicSMemSize, flags)
1422cdef CUresult cuOccupancyMaxPotentialBlockSize(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit) except ?CUDA_ERROR_NOT_FOUND nogil:
1423 return _driver._cuOccupancyMaxPotentialBlockSize(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit) 2RESETEUEVEWEXEYEZE0E1E2E3E4E5E6E7E8E9E!E#E
1426cdef CUresult cuOccupancyMaxPotentialBlockSizeWithFlags(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1427 return _driver._cuOccupancyMaxPotentialBlockSizeWithFlags(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit, flags)
1430cdef CUresult cuOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, CUfunction func, int numBlocks, int blockSize) except ?CUDA_ERROR_NOT_FOUND nogil:
1431 return _driver._cuOccupancyAvailableDynamicSMemPerBlock(dynamicSmemSize, func, numBlocks, blockSize) 2LEMENEOEPEQE
1434cdef CUresult cuOccupancyMaxPotentialClusterSize(int* clusterSize, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1435 return _driver._cuOccupancyMaxPotentialClusterSize(clusterSize, func, config)
1438cdef CUresult cuOccupancyMaxActiveClusters(int* numClusters, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1439 return _driver._cuOccupancyMaxActiveClusters(numClusters, func, config)
1442cdef CUresult cuTexRefSetArray(CUtexref hTexRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1443 return _driver._cuTexRefSetArray(hTexRef, hArray, Flags)
1446cdef CUresult cuTexRefSetMipmappedArray(CUtexref hTexRef, CUmipmappedArray hMipmappedArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1447 return _driver._cuTexRefSetMipmappedArray(hTexRef, hMipmappedArray, Flags)
1450cdef CUresult cuTexRefSetAddress(size_t* ByteOffset, CUtexref hTexRef, CUdeviceptr dptr, size_t bytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1451 return _driver._cuTexRefSetAddress_v2(ByteOffset, hTexRef, dptr, bytes)
1454cdef CUresult cuTexRefSetAddress2D(CUtexref hTexRef, const CUDA_ARRAY_DESCRIPTOR* desc, CUdeviceptr dptr, size_t Pitch) except ?CUDA_ERROR_NOT_FOUND nogil:
1455 return _driver._cuTexRefSetAddress2D_v3(hTexRef, desc, dptr, Pitch)
1458cdef CUresult cuTexRefSetFormat(CUtexref hTexRef, CUarray_format fmt, int NumPackedComponents) except ?CUDA_ERROR_NOT_FOUND nogil:
1459 return _driver._cuTexRefSetFormat(hTexRef, fmt, NumPackedComponents)
1462cdef CUresult cuTexRefSetAddressMode(CUtexref hTexRef, int dim, CUaddress_mode am) except ?CUDA_ERROR_NOT_FOUND nogil:
1463 return _driver._cuTexRefSetAddressMode(hTexRef, dim, am)
1466cdef CUresult cuTexRefSetFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1467 return _driver._cuTexRefSetFilterMode(hTexRef, fm)
1470cdef CUresult cuTexRefSetMipmapFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1471 return _driver._cuTexRefSetMipmapFilterMode(hTexRef, fm)
1474cdef CUresult cuTexRefSetMipmapLevelBias(CUtexref hTexRef, float bias) except ?CUDA_ERROR_NOT_FOUND nogil:
1475 return _driver._cuTexRefSetMipmapLevelBias(hTexRef, bias)
1478cdef CUresult cuTexRefSetMipmapLevelClamp(CUtexref hTexRef, float minMipmapLevelClamp, float maxMipmapLevelClamp) except ?CUDA_ERROR_NOT_FOUND nogil:
1479 return _driver._cuTexRefSetMipmapLevelClamp(hTexRef, minMipmapLevelClamp, maxMipmapLevelClamp)
1482cdef CUresult cuTexRefSetMaxAnisotropy(CUtexref hTexRef, unsigned int maxAniso) except ?CUDA_ERROR_NOT_FOUND nogil:
1483 return _driver._cuTexRefSetMaxAnisotropy(hTexRef, maxAniso)
1486cdef CUresult cuTexRefSetBorderColor(CUtexref hTexRef, float* pBorderColor) except ?CUDA_ERROR_NOT_FOUND nogil:
1487 return _driver._cuTexRefSetBorderColor(hTexRef, pBorderColor)
1490cdef CUresult cuTexRefSetFlags(CUtexref hTexRef, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1491 return _driver._cuTexRefSetFlags(hTexRef, Flags)
1494cdef CUresult cuTexRefGetAddress(CUdeviceptr* pdptr, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1495 return _driver._cuTexRefGetAddress_v2(pdptr, hTexRef)
1498cdef CUresult cuTexRefGetArray(CUarray* phArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1499 return _driver._cuTexRefGetArray(phArray, hTexRef)
1502cdef CUresult cuTexRefGetMipmappedArray(CUmipmappedArray* phMipmappedArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1503 return _driver._cuTexRefGetMipmappedArray(phMipmappedArray, hTexRef)
1506cdef CUresult cuTexRefGetAddressMode(CUaddress_mode* pam, CUtexref hTexRef, int dim) except ?CUDA_ERROR_NOT_FOUND nogil:
1507 return _driver._cuTexRefGetAddressMode(pam, hTexRef, dim)
1510cdef CUresult cuTexRefGetFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1511 return _driver._cuTexRefGetFilterMode(pfm, hTexRef)
1514cdef CUresult cuTexRefGetFormat(CUarray_format* pFormat, int* pNumChannels, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1515 return _driver._cuTexRefGetFormat(pFormat, pNumChannels, hTexRef)
1518cdef CUresult cuTexRefGetMipmapFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1519 return _driver._cuTexRefGetMipmapFilterMode(pfm, hTexRef)
1522cdef CUresult cuTexRefGetMipmapLevelBias(float* pbias, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1523 return _driver._cuTexRefGetMipmapLevelBias(pbias, hTexRef)
1526cdef CUresult cuTexRefGetMipmapLevelClamp(float* pminMipmapLevelClamp, float* pmaxMipmapLevelClamp, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1527 return _driver._cuTexRefGetMipmapLevelClamp(pminMipmapLevelClamp, pmaxMipmapLevelClamp, hTexRef)
1530cdef CUresult cuTexRefGetMaxAnisotropy(int* pmaxAniso, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1531 return _driver._cuTexRefGetMaxAnisotropy(pmaxAniso, hTexRef)
1534cdef CUresult cuTexRefGetBorderColor(float* pBorderColor, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1535 return _driver._cuTexRefGetBorderColor(pBorderColor, hTexRef)
1538cdef CUresult cuTexRefGetFlags(unsigned int* pFlags, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1539 return _driver._cuTexRefGetFlags(pFlags, hTexRef)
1542cdef CUresult cuTexRefCreate(CUtexref* pTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1543 return _driver._cuTexRefCreate(pTexRef)
1546cdef CUresult cuTexRefDestroy(CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1547 return _driver._cuTexRefDestroy(hTexRef)
1550cdef CUresult cuSurfRefSetArray(CUsurfref hSurfRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1551 return _driver._cuSurfRefSetArray(hSurfRef, hArray, Flags)
1554cdef CUresult cuSurfRefGetArray(CUarray* phArray, CUsurfref hSurfRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1555 return _driver._cuSurfRefGetArray(phArray, hSurfRef)
1558cdef 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:
1559 return _driver._cuTexObjectCreate(pTexObject, pResDesc, pTexDesc, pResViewDesc) 2PtUt8hVt9hWtji
1562cdef CUresult cuTexObjectDestroy(CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1563 return _driver._cuTexObjectDestroy(texObject) 2PtUt8hVt9hWtji
1566cdef CUresult cuTexObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1567 return _driver._cuTexObjectGetResourceDesc(pResDesc, texObject)
1570cdef CUresult cuTexObjectGetTextureDesc(CUDA_TEXTURE_DESC* pTexDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1571 return _driver._cuTexObjectGetTextureDesc(pTexDesc, texObject)
1574cdef CUresult cuTexObjectGetResourceViewDesc(CUDA_RESOURCE_VIEW_DESC* pResViewDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1575 return _driver._cuTexObjectGetResourceViewDesc(pResViewDesc, texObject)
1578cdef CUresult cuSurfObjectCreate(CUsurfObject* pSurfObject, const CUDA_RESOURCE_DESC* pResDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
1579 return _driver._cuSurfObjectCreate(pSurfObject, pResDesc) 2StTtji
1582cdef CUresult cuSurfObjectDestroy(CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1583 return _driver._cuSurfObjectDestroy(surfObject) 2StTtji
1586cdef CUresult cuSurfObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1587 return _driver._cuSurfObjectGetResourceDesc(pResDesc, surfObject)
1590cdef 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:
1591 return _driver._cuTensorMapEncodeTiled(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, boxDim, elementStrides, interleave, swizzle, l2Promotion, oobFill)
1594cdef 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:
1595 return _driver._cuTensorMapEncodeIm2col(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCorner, pixelBoxUpperCorner, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, swizzle, l2Promotion, oobFill)
1598cdef 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:
1599 return _driver._cuTensorMapEncodeIm2colWide(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCornerWidth, pixelBoxUpperCornerWidth, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, mode, swizzle, l2Promotion, oobFill)
1602cdef CUresult cuTensorMapReplaceAddress(CUtensorMap* tensorMap, void* globalAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1603 return _driver._cuTensorMapReplaceAddress(tensorMap, globalAddress)
1606cdef CUresult cuDeviceCanAccessPeer(int* canAccessPeer, CUdevice dev, CUdevice peerDev) except ?CUDA_ERROR_NOT_FOUND nogil:
1607 return _driver._cuDeviceCanAccessPeer(canAccessPeer, dev, peerDev)
1610cdef CUresult cuCtxEnablePeerAccess(CUcontext peerContext, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1611 return _driver._cuCtxEnablePeerAccess(peerContext, Flags)
1614cdef CUresult cuCtxDisablePeerAccess(CUcontext peerContext) except ?CUDA_ERROR_NOT_FOUND nogil:
1615 return _driver._cuCtxDisablePeerAccess(peerContext)
1618cdef CUresult cuDeviceGetP2PAttribute(int* value, CUdevice_P2PAttribute attrib, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil:
1619 return _driver._cuDeviceGetP2PAttribute(value, attrib, srcDevice, dstDevice)
1622cdef CUresult cuGraphicsUnregisterResource(CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1623 return _driver._cuGraphicsUnregisterResource(resource) 2!h#h$h@qT5U5V5W5X5(g%h'h$j(h)h*hBAY5Z505
1626cdef CUresult cuGraphicsSubResourceGetMappedArray(CUarray* pArray, CUgraphicsResource resource, unsigned int arrayIndex, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil:
1627 return _driver._cuGraphicsSubResourceGetMappedArray(pArray, resource, arrayIndex, mipLevel)
1630cdef CUresult cuGraphicsResourceGetMappedMipmappedArray(CUmipmappedArray* pMipmappedArray, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1631 return _driver._cuGraphicsResourceGetMappedMipmappedArray(pMipmappedArray, resource)
1634cdef CUresult cuGraphicsResourceGetMappedPointer(CUdeviceptr* pDevPtr, size_t* pSize, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1635 return _driver._cuGraphicsResourceGetMappedPointer_v2(pDevPtr, pSize, resource) 2!h?q#h$h(g%h'h$j(h)h*hKm
1638cdef CUresult cuGraphicsResourceSetMapFlags(CUgraphicsResource resource, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1639 return _driver._cuGraphicsResourceSetMapFlags_v2(resource, flags)
1642cdef CUresult cuGraphicsMapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1643 return _driver._cuGraphicsMapResources(count, resources, hStream) 2!h?q#h$h(g%h'h$j(h)h*hKm
1646cdef CUresult cuGraphicsUnmapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1647 return _driver._cuGraphicsUnmapResources(count, resources, hStream) 2!h#h$h(g%h'h$j(h)h*hKmBA
1650cdef CUresult cuGetProcAddress(const char* symbol, void** pfn, int cudaVersion, cuuint64_t flags, CUdriverProcAddressQueryResult* symbolStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
1651 return _driver._cuGetProcAddress_v2(symbol, pfn, cudaVersion, flags, symbolStatus)
1654cdef CUresult cuCoredumpGetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1655 return _driver._cuCoredumpGetAttribute(attrib, value, size)
1658cdef CUresult cuCoredumpGetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1659 return _driver._cuCoredumpGetAttributeGlobal(attrib, value, size) 215
1662cdef CUresult cuCoredumpSetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1663 return _driver._cuCoredumpSetAttribute(attrib, value, size)
1666cdef CUresult cuCoredumpSetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1667 return _driver._cuCoredumpSetAttributeGlobal(attrib, value, size) 215
1670cdef CUresult cuGetExportTable(const void** ppExportTable, const CUuuid* pExportTableId) except ?CUDA_ERROR_NOT_FOUND nogil:
1671 return _driver._cuGetExportTable(ppExportTable, pExportTableId)
1674cdef CUresult cuGreenCtxCreate(CUgreenCtx* phCtx, CUdevResourceDesc desc, CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1675 return _driver._cuGreenCtxCreate(phCtx, desc, dev, flags) 2MmWkXk/e# $ YkZk0k1k2k3k
1678cdef CUresult cuGreenCtxDestroy(CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1679 return _driver._cuGreenCtxDestroy(hCtx) 2Mm_G`G{G# $ |G}G~GaHbHcH
1682cdef CUresult cuCtxFromGreenCtx(CUcontext* pContext, CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1683 return _driver._cuCtxFromGreenCtx(pContext, hCtx) 2MmWkXk/e# $ YkZk0k1k2k3k
1686cdef CUresult cuDeviceGetDevResource(CUdevice device, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1687 return _driver._cuDeviceGetDevResource(device, resource, type) 22535:BWkXk/e_n`nYkZk0k1k2k3k;B=B?B@B[B]B^B_B`B{B|B}B~BaCbCcCdCeCfCgChC
1690cdef CUresult cuCtxGetDevResource(CUcontext hCtx, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1691 return _driver._cuCtxGetDevResource(hCtx, resource, type)
1694cdef CUresult cuGreenCtxGetDevResource(CUgreenCtx hCtx, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1695 return _driver._cuGreenCtxGetDevResource(hCtx, resource, type) 2MmZ9mA
1698cdef CUresult cuDevSmResourceSplitByCount(CUdevResource* result, unsigned int* nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, unsigned int minCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1699 return _driver._cuDevSmResourceSplitByCount(result, nbGroups, input, remainder, flags, minCount) 235
1702cdef CUresult cuDevResourceGenerateDesc(CUdevResourceDesc* phDesc, CUdevResource* resources, unsigned int nbResources) except ?CUDA_ERROR_NOT_FOUND nogil:
1703 return _driver._cuDevResourceGenerateDesc(phDesc, resources, nbResources) 2MmWkXk/e# $ YkZk0k1k2k3k
1706cdef CUresult cuGreenCtxRecordEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1707 return _driver._cuGreenCtxRecordEvent(hCtx, hEvent)
1710cdef CUresult cuGreenCtxWaitEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1711 return _driver._cuGreenCtxWaitEvent(hCtx, hEvent)
1714cdef CUresult cuStreamGetGreenCtx(CUstream hStream, CUgreenCtx* phCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1715 return _driver._cuStreamGetGreenCtx(hStream, phCtx)
1718cdef CUresult cuGreenCtxStreamCreate(CUstream* phStream, CUgreenCtx greenCtx, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil:
1719 return _driver._cuGreenCtxStreamCreate(phStream, greenCtx, flags, priority) 2mA*b# $ p5|N?j
1722cdef CUresult cuLogsRegisterCallback(CUlogsCallback callbackFunc, void* userData, CUlogsCallbackHandle* callback_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1723 return _driver._cuLogsRegisterCallback(callbackFunc, userData, callback_out)
1726cdef CUresult cuLogsUnregisterCallback(CUlogsCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
1727 return _driver._cuLogsUnregisterCallback(callback)
1730cdef CUresult cuLogsCurrent(CUlogIterator* iterator_out, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1731 return _driver._cuLogsCurrent(iterator_out, flags)
1734cdef CUresult cuLogsDumpToFile(CUlogIterator* iterator, const char* pathToFile, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1735 return _driver._cuLogsDumpToFile(iterator, pathToFile, flags)
1738cdef CUresult cuLogsDumpToMemory(CUlogIterator* iterator, char* buffer, size_t* size, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1739 return _driver._cuLogsDumpToMemory(iterator, buffer, size, flags)
1742cdef CUresult cuCheckpointProcessGetRestoreThreadId(int pid, int* tid) except ?CUDA_ERROR_NOT_FOUND nogil:
1743 return _driver._cuCheckpointProcessGetRestoreThreadId(pid, tid)
1746cdef CUresult cuCheckpointProcessGetState(int pid, CUprocessState* state) except ?CUDA_ERROR_NOT_FOUND nogil:
1747 return _driver._cuCheckpointProcessGetState(pid, state) 209
1750cdef CUresult cuCheckpointProcessLock(int pid, CUcheckpointLockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1751 return _driver._cuCheckpointProcessLock(pid, args)
1754cdef CUresult cuCheckpointProcessCheckpoint(int pid, CUcheckpointCheckpointArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1755 return _driver._cuCheckpointProcessCheckpoint(pid, args)
1758cdef CUresult cuCheckpointProcessRestore(int pid, CUcheckpointRestoreArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1759 return _driver._cuCheckpointProcessRestore(pid, args)
1762cdef CUresult cuCheckpointProcessUnlock(int pid, CUcheckpointUnlockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1763 return _driver._cuCheckpointProcessUnlock(pid, args)
1766cdef CUresult cuGraphicsEGLRegisterImage(CUgraphicsResource* pCudaResource, EGLImageKHR image, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1767 return _driver._cuGraphicsEGLRegisterImage(pCudaResource, image, flags)
1770cdef CUresult cuEGLStreamConsumerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream) except ?CUDA_ERROR_NOT_FOUND nogil:
1771 return _driver._cuEGLStreamConsumerConnect(conn, stream)
1774cdef CUresult cuEGLStreamConsumerConnectWithFlags(CUeglStreamConnection* conn, EGLStreamKHR stream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1775 return _driver._cuEGLStreamConsumerConnectWithFlags(conn, stream, flags)
1778cdef CUresult cuEGLStreamConsumerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1779 return _driver._cuEGLStreamConsumerDisconnect(conn)
1782cdef CUresult cuEGLStreamConsumerAcquireFrame(CUeglStreamConnection* conn, CUgraphicsResource* pCudaResource, CUstream* pStream, unsigned int timeout) except ?CUDA_ERROR_NOT_FOUND nogil:
1783 return _driver._cuEGLStreamConsumerAcquireFrame(conn, pCudaResource, pStream, timeout)
1786cdef CUresult cuEGLStreamConsumerReleaseFrame(CUeglStreamConnection* conn, CUgraphicsResource pCudaResource, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1787 return _driver._cuEGLStreamConsumerReleaseFrame(conn, pCudaResource, pStream)
1790cdef CUresult cuEGLStreamProducerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream, EGLint width, EGLint height) except ?CUDA_ERROR_NOT_FOUND nogil:
1791 return _driver._cuEGLStreamProducerConnect(conn, stream, width, height)
1794cdef CUresult cuEGLStreamProducerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1795 return _driver._cuEGLStreamProducerDisconnect(conn)
1798cdef CUresult cuEGLStreamProducerPresentFrame(CUeglStreamConnection* conn, CUeglFrame eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1799 return _driver._cuEGLStreamProducerPresentFrame(conn, eglframe, pStream)
1802cdef CUresult cuEGLStreamProducerReturnFrame(CUeglStreamConnection* conn, CUeglFrame* eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1803 return _driver._cuEGLStreamProducerReturnFrame(conn, eglframe, pStream)
1806cdef CUresult cuGraphicsResourceGetMappedEglFrame(CUeglFrame* eglFrame, CUgraphicsResource resource, unsigned int index, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil:
1807 return _driver._cuGraphicsResourceGetMappedEglFrame(eglFrame, resource, index, mipLevel)
1810cdef CUresult cuEventCreateFromEGLSync(CUevent* phEvent, EGLSyncKHR eglSync, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1811 return _driver._cuEventCreateFromEGLSync(phEvent, eglSync, flags)
1814cdef CUresult cuGraphicsGLRegisterBuffer(CUgraphicsResource* pCudaResource, GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1815 return _driver._cuGraphicsGLRegisterBuffer(pCudaResource, buffer, Flags) 2!h?q#h$h@qT5U5V5W5X5(g%h'h$jLO(h)hMO*hKmBAY5Z505
1818cdef CUresult cuGraphicsGLRegisterImage(CUgraphicsResource* pCudaResource, GLuint image, GLenum target, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1819 return _driver._cuGraphicsGLRegisterImage(pCudaResource, image, target, Flags) 2KO
1822cdef CUresult cuGLGetDevices(unsigned int* pCudaDeviceCount, CUdevice* pCudaDevices, unsigned int cudaDeviceCount, CUGLDeviceList deviceList) except ?CUDA_ERROR_NOT_FOUND nogil:
1823 return _driver._cuGLGetDevices_v2(pCudaDeviceCount, pCudaDevices, cudaDeviceCount, deviceList)
1826cdef CUresult cuGLCtxCreate(CUcontext* pCtx, unsigned int Flags, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
1827 return _driver._cuGLCtxCreate_v2(pCtx, Flags, device)
1830cdef CUresult cuGLInit() except ?CUDA_ERROR_NOT_FOUND nogil:
1831 return _driver._cuGLInit()
1834cdef CUresult cuGLRegisterBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1835 return _driver._cuGLRegisterBufferObject(buffer)
1838cdef CUresult cuGLMapBufferObject(CUdeviceptr* dptr, size_t* size, GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1839 return _driver._cuGLMapBufferObject_v2(dptr, size, buffer)
1842cdef CUresult cuGLUnmapBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1843 return _driver._cuGLUnmapBufferObject(buffer)
1846cdef CUresult cuGLUnregisterBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1847 return _driver._cuGLUnregisterBufferObject(buffer)
1850cdef CUresult cuGLSetBufferObjectMapFlags(GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1851 return _driver._cuGLSetBufferObjectMapFlags(buffer, Flags)
1854cdef CUresult cuGLMapBufferObjectAsync(CUdeviceptr* dptr, size_t* size, GLuint buffer, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1855 return _driver._cuGLMapBufferObjectAsync_v2(dptr, size, buffer, hStream)
1858cdef CUresult cuGLUnmapBufferObjectAsync(GLuint buffer, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1859 return _driver._cuGLUnmapBufferObjectAsync(buffer, hStream)
1862cdef CUresult cuProfilerInitialize(const char* configFile, const char* outputFile, CUoutput_mode outputMode) except ?CUDA_ERROR_NOT_FOUND nogil:
1863 return _driver._cuProfilerInitialize(configFile, outputFile, outputMode)
1866cdef CUresult cuProfilerStart() except ?CUDA_ERROR_NOT_FOUND nogil:
1867 return _driver._cuProfilerStart() 245
1870cdef CUresult cuProfilerStop() except ?CUDA_ERROR_NOT_FOUND nogil:
1871 return _driver._cuProfilerStop() 245
1874cdef CUresult cuVDPAUGetDevice(CUdevice* pDevice, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1875 return _driver._cuVDPAUGetDevice(pDevice, vdpDevice, vdpGetProcAddress)
1878cdef CUresult cuVDPAUCtxCreate(CUcontext* pCtx, unsigned int flags, CUdevice device, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1879 return _driver._cuVDPAUCtxCreate_v2(pCtx, flags, device, vdpDevice, vdpGetProcAddress)
1882cdef CUresult cuGraphicsVDPAURegisterVideoSurface(CUgraphicsResource* pCudaResource, VdpVideoSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1883 return _driver._cuGraphicsVDPAURegisterVideoSurface(pCudaResource, vdpSurface, flags)
1886cdef CUresult cuGraphicsVDPAURegisterOutputSurface(CUgraphicsResource* pCudaResource, VdpOutputSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1887 return _driver._cuGraphicsVDPAURegisterOutputSurface(pCudaResource, vdpSurface, flags)
1890cdef CUresult cuDeviceGetHostAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
1891 return _driver._cuDeviceGetHostAtomicCapabilities(capabilities, operations, count, dev)
1894cdef CUresult cuCtxGetDevice_v2(CUdevice* device, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1895 return _driver._cuCtxGetDevice_v2(device, ctx)
1898cdef CUresult cuCtxSynchronize_v2(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1899 return _driver._cuCtxSynchronize_v2(ctx)
1902cdef 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:
1903 return _driver._cuMemcpyBatchAsync_v2(dsts, srcs, sizes, count, attrs, attrsIdxs, numAttrs, hStream)
1906cdef CUresult cuMemcpy3DBatchAsync(size_t numOps, CUDA_MEMCPY3D_BATCH_OP* opList, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1907 return _driver._cuMemcpy3DBatchAsync_v2(numOps, opList, flags, hStream)
1910cdef CUresult cuMemGetDefaultMemPool(CUmemoryPool* pool_out, CUmemLocation* location, CUmemAllocationType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1911 return _driver._cuMemGetDefaultMemPool(pool_out, location, type)
1914cdef CUresult cuMemGetMemPool(CUmemoryPool* pool, CUmemLocation* location, CUmemAllocationType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1915 return _driver._cuMemGetMemPool(pool, location, type) 2(r)r;rXnrk%dYnskZntk@r[r]r^r_r`r{rumdddxvmexPiQiRifxRb/dwm;gCEedDE=gEE?gFE@gGE[gHEfdIE]gJE_ggd!jxm
1918cdef CUresult cuMemSetMemPool(CUmemLocation* location, CUmemAllocationType type, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
1919 return _driver._cuMemSetMemPool(location, type, pool)
1922cdef 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:
1923 return _driver._cuMemPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 2+gYe,g-g
1926cdef CUresult cuMemDiscardBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1927 return _driver._cuMemDiscardBatchAsync(dptrs, sizes, count, flags, hStream) 2+g1m2m
1930cdef 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:
1931 return _driver._cuMemDiscardAndPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 2Ye%d
1934cdef CUresult cuDeviceGetP2PAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil:
1935 return _driver._cuDeviceGetP2PAtomicCapabilities(capabilities, operations, count, srcDevice, dstDevice)
1938cdef CUresult cuGreenCtxGetId(CUgreenCtx greenCtx, unsigned long long* greenCtxId) except ?CUDA_ERROR_NOT_FOUND nogil:
1939 return _driver._cuGreenCtxGetId(greenCtx, greenCtxId)
1942cdef 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:
1943 return _driver._cuMulticastBindMem_v2(mcHandle, dev, mcOffset, memHandle, memOffset, size, flags)
1946cdef 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:
1947 return _driver._cuMulticastBindAddr_v2(mcHandle, dev, mcOffset, memptr, size, flags)
1950cdef CUresult cuGraphNodeGetContainingGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1951 return _driver._cuGraphNodeGetContainingGraph(hNode, phGraph) 2iu
1954cdef CUresult cuGraphNodeGetLocalId(CUgraphNode hNode, unsigned int* nodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
1955 return _driver._cuGraphNodeGetLocalId(hNode, nodeId) 2DA
1958cdef CUresult cuGraphNodeGetToolsId(CUgraphNode hNode, unsigned long long* toolsNodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
1959 return _driver._cuGraphNodeGetToolsId(hNode, toolsNodeId) 2EA
1962cdef CUresult cuGraphGetId(CUgraph hGraph, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1963 return _driver._cuGraphGetId(hGraph, graphId) 2hO
1966cdef CUresult cuGraphExecGetId(CUgraphExec hGraphExec, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1967 return _driver._cuGraphExecGetId(hGraphExec, graphId) 2@j
1970cdef 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:
1971 return _driver._cuDevSmResourceSplit(result, nbGroups, input, remainder, flags, groupParams) 225MmWkXk/e# $ YkZk0k1k2k3k19293949596979
1974cdef CUresult cuStreamGetDevResource(CUstream hStream, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1975 return _driver._cuStreamGetDevResource(hStream, resource, type) 2eO
1978cdef CUresult cuKernelGetParamCount(CUkernel kernel, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1979 return _driver._cuKernelGetParamCount(kernel, paramCount)
1982cdef CUresult cuMemcpyWithAttributesAsync(CUdeviceptr dst, CUdeviceptr src, size_t size, CUmemcpyAttributes* attr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1983 return _driver._cuMemcpyWithAttributesAsync(dst, src, size, attr, hStream)
1986cdef CUresult cuMemcpy3DWithAttributesAsync(CUDA_MEMCPY3D_BATCH_OP* op, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1987 return _driver._cuMemcpy3DWithAttributesAsync(op, flags, hStream)
1990cdef CUresult cuStreamBeginCaptureToCig(CUstream hStream, CUstreamCigCaptureParams* streamCigCaptureParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1991 return _driver._cuStreamBeginCaptureToCig(hStream, streamCigCaptureParams)
1994cdef CUresult cuStreamEndCaptureToCig(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1995 return _driver._cuStreamEndCaptureToCig(hStream)
1998cdef CUresult cuFuncGetParamCount(CUfunction func, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1999 return _driver._cuFuncGetParamCount(func, paramCount)
2002cdef CUresult cuLaunchHostFunc_v2(CUstream hStream, CUhostFn fn, void* userData, unsigned int syncMode) except ?CUDA_ERROR_NOT_FOUND nogil:
2003 return _driver._cuLaunchHostFunc_v2(hStream, fn, userData, syncMode)
2006cdef CUresult cuGraphNodeGetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
2007 return _driver._cuGraphNodeGetParams(hNode, nodeParams) 2YdZd0d1d2d3d4d5d(j
2010cdef CUresult cuCoredumpRegisterStartCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
2011 return _driver._cuCoredumpRegisterStartCallback(callback, userData, callbackOut)
2014cdef CUresult cuCoredumpRegisterCompleteCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
2015 return _driver._cuCoredumpRegisterCompleteCallback(callback, userData, callbackOut)
2018cdef CUresult cuCoredumpDeregisterStartCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
2019 return _driver._cuCoredumpDeregisterStartCallback(callback)
2022cdef CUresult cuCoredumpDeregisterCompleteCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
2023 return _driver._cuCoredumpDeregisterCompleteCallback(callback)
2026cdef CUresult cuLogicalEndpointIdReserve(CUlogicalEndpointId* baseLeId, cuuint32_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
2027 return _driver._cuLogicalEndpointIdReserve(baseLeId, count)
2030cdef CUresult cuLogicalEndpointIdRelease(CUlogicalEndpointId baseLeId, cuuint32_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
2031 return _driver._cuLogicalEndpointIdRelease(baseLeId, count)
2034cdef CUresult cuLogicalEndpointCreate(CUlogicalEndpointId leId, const CUlogicalEndpointProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
2035 return _driver._cuLogicalEndpointCreate(leId, prop)
2038cdef CUresult cuLogicalEndpointAddDevice(CUlogicalEndpointId leId, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
2039 return _driver._cuLogicalEndpointAddDevice(leId, dev)
2042cdef CUresult cuLogicalEndpointDestroy(CUlogicalEndpointId leId) except ?CUDA_ERROR_NOT_FOUND nogil:
2043 return _driver._cuLogicalEndpointDestroy(leId)
2046cdef CUresult cuLogicalEndpointBindAddr(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, void* ptr, cuuint64_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
2047 return _driver._cuLogicalEndpointBindAddr(leId, dev, offset, ptr, size, flags)
2050cdef 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:
2051 return _driver._cuLogicalEndpointBindMem(leId, dev, offset, memHandle, memOffset, size, flags)
2054cdef CUresult cuLogicalEndpointUnbind(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, cuuint64_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
2055 return _driver._cuLogicalEndpointUnbind(leId, dev, offset, size)
2058cdef CUresult cuLogicalEndpointExport(void* handle, CUlogicalEndpointId leId, CUlogicalEndpointIpcHandleType handleType) except ?CUDA_ERROR_NOT_FOUND nogil:
2059 return _driver._cuLogicalEndpointExport(handle, leId, handleType)
2062cdef CUresult cuLogicalEndpointImport(CUlogicalEndpointId leId, const void* handle, CUlogicalEndpointIpcHandleType handleType) except ?CUDA_ERROR_NOT_FOUND nogil:
2063 return _driver._cuLogicalEndpointImport(leId, handle, handleType)
2066cdef CUresult cuLogicalEndpointGetLimits(cuuint64_t* bindAlignment, cuuint64_t* maxSize, const CUlogicalEndpointProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
2067 return _driver._cuLogicalEndpointGetLimits(bindAlignment, maxSize, prop)
2070cdef CUresult cuLogicalEndpointQuery(CUlogicalEndpointId leId, cuuint32_t count, int* queryStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
2071 return _driver._cuLogicalEndpointQuery(leId, count, queryStatus)
2074cdef CUresult cuStreamBeginRecaptureToGraph(CUstream hStream, CUstreamCaptureMode mode, CUgraph hGraph, CUgraphRecaptureCallback callbackFunc, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil:
2075 return _driver._cuStreamBeginRecaptureToGraph(hStream, mode, hGraph, callbackFunc, userData)