Coverage for cuda/bindings/cydriver.pyx: 67.06%
1029 statements
« prev ^ index » next coverage.py v7.14.1, created at 2026-06-13 01:38 +0000
« prev ^ index » next coverage.py v7.14.1, created at 2026-06-13 01:38 +0000
1# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved.
2#
3# SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE
4#
5# This code was automatically generated across versions from 12.9.0 to 13.3.0, generator version 0.3.1.dev1622+g48467ab08.d20260421. Do not modify it directly.
7from ._internal cimport driver as _driver
9cdef CUresult cuGetErrorString(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil:
10 return _driver._cuGetErrorString(error, pStr) 2aMkybM
13cdef CUresult cuGetErrorName(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil:
14 return _driver._cuGetErrorName(error, pStr) 2;rAl=rBlCl=bDlaMkybMdZ} Hh|i
17cdef CUresult cuInit(unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
18 return _driver._cuInit(Flags) 2a ly?rmynyoypyqyrysytyuyvywyxyyyzyAyByCy@r[r]r^r_r`r{r^p|r}r~rasbscsdsesfsgshsisjskslsmsnsospsqsDyEyFyGyHyIyJyKyLyMyNyOyPyQyRySy?beZTyUyVyWy
21cdef CUresult cuDriverGetVersion(int* driverVersion) except ?CUDA_ERROR_NOT_FOUND nogil:
22 return _driver._cuDriverGetVersion(driverVersion) 2a fZgZhZiZjZkZ
25cdef CUresult cuDeviceGet(CUdevice* device, int ordinal) except ?CUDA_ERROR_NOT_FOUND nogil:
26 return _driver._cuDeviceGet(device, ordinal) 2lymynyoypyqyrysytyuyvywyxyyyzyAykyByCy@r[r]r^r_r`r{r^p|r}r~rasbscsdsesfsgshsisjskslsmsnsospsqsDyEyFyGyHyIyJyKyLyMyNyOyPyQyRySyTyUyVyWy
29cdef CUresult cuDeviceGetCount(int* count) except ?CUDA_ERROR_NOT_FOUND nogil:
30 return _driver._cuDeviceGetCount(count) 2a rscMdMeMfMgMhMiMjMkMlMmMnMoMpMqMrMsMtMuMvMwMxMyMzMAMBMCMDMEMFMGMHMIMXyYyZy0ylZ1y2y3y4y5yEl}iFl6y~iGlHl7y8y9y!y#yJM$y%y'y(y)y*y+y,y-y.y/y:y;y=y?y@y[y]y^y_y`y{y|y}y~yazbzczdzezfzgzhzizIlJl@baj{d|dbjKlLlMlNlod}dIhJhKhLhOlPlQlRl[bcj~daedjSlTlUlVlpdbeMhNhOhPhWlXlYlejZljzfj0l1l2lgj3lhj4l5l6l7l]bijcedejj8l9l!l#lqdeeQhRhShTh$l%l'l(l^bkjfegelj)l*l+l,lrdheUhVhWhXh-l.l/l:l_bmjiejenj;l=l?l@lsdkeYhZh0h1h[l]l^l_l`bojlemepj`l{l|l}ltdne2h3h4h5h~lambmqjcmrjdmemfmsjgmtjhmimKMjmujkmvjlmmmLMMMNMOMPMQMRMSMTMUMVMWMXMYMZM0M1M2M3M4M5M6M7M8M9M!M#M$M%M'M(M)M*M~ +M,M-M.M/M:M;M=M?M@M[M]M^M_M`M{M|M}M~MaNbNcNdNeNfNgNhNiNkzjNkNlNmNnNoNpNqN_p`prNss{pnm|p}p~paqbqsNomwjtspmxjqmyjuscqdqeqfqgqhqiqjqtNuNlzmznzoeozkqpzqzperzqezjsz% vsgghgtzuzvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzlqrermmqigQbmZabbb+ RbSbse6hnqAjcbdbebfbwsgbhb?rvNwNxNyNzNANBNCNDNxsyszsAsBsCsDsEsFsGsHsIsJsKsLsTc0 UcENsmFNGNHNINJNKNLNMNNNONPNjgTzBjCjtetmumDjEjFjQNGjHjIjUzVzWzXzYzZz0z1z2z3z4z5z6z7z8z9z!z#zRNueSNVcWcXcYcMsNsOsPsQsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s%s's(s)s*s+s,s-s{bkglgoqpq.s/s:s;s=s?s@s[s]s^s_s`s{s|s}s~satbtctdtetftgthtitjtktltmtntotptqtrtstttutvt$z%zTb'zwt|bTN7hUN8h9hVNWNibud(z!hXNveYNvd}b#hweZN$hxe%hye'hzewd~b(hmgngZc0Nog1Npgqg2Nrg3Nxdsg)h4NAe5Nyd6Nac*hBe7N+hCe,h8NDe9N-hEe!Nzd#Nbc.hFetgug$N/hAd%N0c'NBdJjxtvmccCdUbdcGewm(N:h;h} )NqqnZ*Nxmym+Nzm,NAmBmCmM -NDmHh.N/N:N;N=N?N@N[N]N^NEmFmGmHmytztAtBtCtDtEtFtGtImJmKmLmMmNmOmPmQmRmSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!m#m$m%m'm(m)m*m+m,m-m.m/m:m;m=m?m@m[m]m^m_m`m{m|m}m~manbncndnenfngnhninjnknlnmnKjecrq_N`NLj)zMjNjOj*znnonpnqnHeIe=hsq+zHtrnsnPjtnItunQjfctq{N,zRj-zSjTjUj.zvnwnxnynJeKe?huq/zJtznAnVbLeMeVjvgwgxgDdNe@hygzgOe' PeEd1c2c3c[hFdGdHdQeWbWjXb4cAg]hIdJdjbkbYb, - . / ^hlbBgCgDgEg_hBnCn5cKdFgvqDnEnXjgcwqYjZj0j1j:zFnGnHnInRe|NSe`hxq;zJnKn2j{hZbLn=z|hKt}h~haiLt3j4j5j6jLd?zMdGgMnMtyq7j8j9jmbNdOdbiTeUeVe6cWeHgXeYeci0bNn@zdi!j#jeiNt$j%j'j(jPd[zQdIgOnOt)j*jfigiZe0e1e2ehi3e4e5e6enbRdSd7e8e9eTdJg!e#ePnhczq+j,j-j.jQnRnSn$e%eii]zTnUnKgLgMgNgVnWnXnYnZnjiicOgPgUdVdQg/j'e(e)e*e7c+e:j,e-ejc8c9c!cWdkclcobmcncoc0npcAq;j=j?j@j^z1n2n3n4n.e/ekiBq_z5n6n3 1b2bqc#c$c%c'c: (c)cXd:e;eYd=e?e[jrclimi@e[eni7nRgSgTg8n]eZdUg9nVgWg!nsc]j^j_j`j#n$n%n^e_eoi'n(npiXgpb{jPtYgCqZg0g1gDqqirisi*cQt+c`e|jEqtiui)n*n}jtcFq}N~N~j`zakbkck{z+n,n-n.n{e|eviGq|zRt/n:n3b}e~edk2g3g4g0dafwi5g6gbf( cf1d,c2dxi3d4d5ddf4bek5b-cyizi6d7dqbrb6b; = ? @ Aisb7g8g9g!gBi;n=n.c8d#gHq?n@n[nfkucIqgkhkikjk}z]n^n_n`nefaOffCiSt~z{n|n}nkkvcJqbOlkaAmknkokbA~naobocogfcOhfDiTtcAUtdoeopktb9d!dEiifjfkf/clf$gmfnfqkFi7bfodAGirkskHiVttkukvkwk#deA$d%gKqWtxkykIiJiofpfqfrfKisftfufvfub%d'dwfxfyf(d'gzfAfgowcLqzkAkBkCkhoiojoBfCfLifAkolo(g)g*g+gmonooopoqoMixc,g-g)d*d.gDkDfEfFfGf:cHfEkIfJfyc;c=c?c+dzcAcvbBcCcDcroEcMqFkGkHkIkgAsotouovoKfLfNiXthAwoxo4 8b9bFc@c[c]c^c[ _c`c,dMfNf-dOfPfyoGcJkKk/g:gLkNqOiPiQizoQfRfRiOqSiTiAoHcMkNkOkPkBoCoDoSfTfUiEoFoVi;gwbQkYt=gPq?g@g[gQqWiXiYiZi{cZt|cUfGoRq0i1iHodOeO}c?b.d/d0t1tIoRkIcSqfOiASkjATkUkVkkAJoKoLoMoVfWf2iTqUqgO2t3thOlA4tNoOoPoWkJcVqiOjOXkmAYkZk0knAQoRoSoToXfYf3iWqoA5tUoVoWo1kKcXqkOpA2kqA3k4k5krAXoYoZo0oZf0f4iYqsA6t1o2o3o6kLcZqlOtA7kuA8k9k!kvA4o5o6o7o1f2f5i0qwA7t8o9o!o#kMc1qmOxA$kyA%k'k(kzA#o$o%o'o3f4f6i2qAA8t(o)o*o)kNc3qnOBA*kCA+k,k-kDA+o,o-o.o5f6f7i4qEA9t/o:o;o.kOc5qoOpO/kFA:k;k=kGA=o?o@o[o7f8f8i!t#tHA$t]o^o_o?kPc6qqOrO@kIA[k]k^kJA`o{o|o9f!f9i%t'tKA(t}o~osOtO)tuOvOwOxOyOzOAOBOCODOEOFOGOHOIOJOKOLOMONOOOPOQOROSOTOUOVOWOXOYOZO*t+t|i0O1O2O3O4O5O6O7O8O9O!O,t-t.t/t:t;t=t?t@t[t]t#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~OaPbPcPdPePfPgPhPiPjP^t_t`t{t|t}t~taubucudueufuguhuiujukulumunuoupuqurusutuuuvuwuxuyuzuAuBuCuDuEukPlPmPFuGuHunPoPpPqPrPsPtPuPvPwPxPyP#f$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}fzPAPBPCPDPEPFPGPHPIPJPKPLPMPNPOPPPQPRPSPTPUP
33cdef CUresult cuDeviceGetName(char* name, int len, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
34 return _driver._cuDeviceGetName(name, len, dev) 2nmuNoZapoekqIupeqe% ] bp]g!i#icpdpepfpgghglqreJuKumqLuigQbabbb+ ~fRbSbse6hnq7q?rVPLAiA
37cdef CUresult cuDeviceGetUuid(CUuuid* uuid, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
38 return _driver._cuDeviceGetUuid_v2(uuid, dev) 2nm}pzjvs8qgprm9qAjwsvNpZqZrZsZtZMANAve}bwexeyeze~bmgAeacBeCeDeEebcFetgdc:h;hOA,z2j{hZbLn=z|hKt}h~haiLt3j4j5j6jLd?zMdGgMnMtyq7j8j}c?b.d/dpAtAxABA
41cdef CUresult cuDeviceGetLuid(char* luid, unsigned int* deviceNodeMask, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
42 return _driver._cuDeviceGetLuid(luid, deviceNodeMask, dev)
45cdef CUresult cuDeviceTotalMem(size_t* bytes, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
46 return _driver._cuDeviceTotalMem_v2(bytes, dev)
49cdef CUresult cuDeviceGetTexture1DLinearMaxWidth(size_t* maxWidthInElements, CUarray_format format, unsigned numChannels, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
50 return _driver._cuDeviceGetTexture1DLinearMaxWidth(maxWidthInElements, format, numChannels, dev)
53cdef CUresult cuDeviceGetAttribute(int* pi, CUdevice_attribute attrib, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
54 return _driver._cuDeviceGetAttribute(pi, attrib, dev) 2a rsS T 5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J PAQA!q;rMuRANuEl}iFl~iGlHl#q~cadbd:d2 uZvZybzbAb!bBb6 7 8 * #b$b%bQcwZ$q%q'q(q)q*q$i_kIlJl@baj{d|dbjod}dIhJhKhLhQlRl[bcj~daedjpdbeMhNhOhPhYlejZlfj0l1l2lgj3lhj4l5l6l7l]bijcedejjqdeeQhRhShTh'l(l^bkjfegeljrdheUhVhWhXh/l:l_bmjiejenjsdkeYhZh0h1h^l_l`bojlemepjtdne2h3h4h5hbmqjcmrjdmemfmsjgmtjhmimjmujkmvjlmmmxZ`k+q;dyZcdzZWPXPYPZP0P1PCbDbEbFb'b=d?dK N ,qagX ^ _ (bO L A B b 9 kzw E Y Z Gb)b*bddU _p`p{p|p~paqbq-qomwjtspmxjqmyjuscqdqOueqfqgqhqiqjqzj% ] .qvs8q/qgprm:q9q;qAjws?rhpSATA^g_gxsUAVAWAXAYAZA0A1A2Ays3A4Azs5A6A7A8A9A!A#A$A%AAs'A(A)A*A+A,A-A.A/ABs:A;A=A?A@A[A]A^A_ACs`A{A|A}A~AaBbBDscBdBeBfBgBhBiBjBkBlBmBnBEsoBpBFsqBrBsBtBuBvBwBxByBzBABBBCBGsDBEBFBHsGBHBIBJBKBIsLBMBNBOBPBQBRBSBTBUBVBWBXBYBZB0B1B2B3B4B5B6B7B8B9B!B#B$BJs%B'B(BKs)BLs*B+B,B-B.B/B:B;B=B?B@B[B]B^B_B0 ` RcHbteV tmW umAZBZIb@d[d%i'i(ibg)i*i]d2PVcWcXcYcMsNsOsPsQsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s%s's(s)s*s+s`B,s-skglg+i,i%zTb'z3P{k|bPu|kQu7h8h9hRuib-iud}k!hvevd}b#hwe$hxe%hye'hzewd~b(hng{BZc|Bog}Bpg~BqgaCrgbCcCsgdC)hAeydac*hBe+hCe,hDe-hEezdbc.hFetgug/hAd0cBd4PCd.i~kUbdcGewm:h;h5Pedfd} 6Pgdqq7Pxmym=qzm?qAmBmCmM DmHh@q[q]q^q_q`q{q|q}q~qEmFmGmHmytztAtBtCtDtEtFtGteCImfCJmgCKmhCLmiCMmjCNmSuOmTuPmUuQmVuRmWuSmXuTmYuUmZuVm0uWm1uXm2uYm3uZm4u0m5u1m6u2m7u3m8u4m9u5m6m7mkC8mlC9mmC!mnC#moC$mpC%mqC'mrC(msC)mtC*muC+mvC,mwC-mxC.myC/mzC:mAC;mBC=mCC?mDC@mEC[m]m^m_m`m{m|m}m~manbncndnenfngnhnOAmnKjecLjOjqnHeIe=hsqPjtnunQjfcRjUjynJeKe?huqVbLeMeVjvgwgxgDdNe@hygzgOe' PeEd1c2c3c[hFdGdHdQeWbWjXb4cAg]hIdJdjbkbYb, - . / ^hlbBgEg5cKdFgEnXjgcYj1jInReSe`hxq2j{hZb|hai6jLdMdGgMn9jmbNdOdbiTeUeVe6cWeHgXeYeci0bdiei(jPdQdIgOnnbRdSd7e8e9eTdJg!e#ePnhc+j.j$e%eiijiicOgPgUdVdQg/j'e(e)e*e7c+e:j,e-ejc8c9c!cWdkclcobmcncoc0npc;j@j4n.e/ekiBq3 1b2bqc#c$c%c'c: (c)cXd:e;eYd=e?e[jrclimi@e[eni7nRgSgTg8n]eZdUg9nVgWg!nsc]j`j^e_eoipiXgpbYg1gsi*c+c`e|j*n}jtc~jck.n{e|eviGq3b}e~edk2g3g4g0dafwi5g6gbf( cf1d^d,c2dxi3d4d5ddf4bek5b-cyizi6d7dqbrb6b; = ? @ Aisb7g!g.c8d#g[nfkucgkjk`nefffCiSt}nkkvclkokcogfhfDiTtpktb9d!dEiifjfkf/clf$gmfnfqkFi7bGiHiwk#d$d%gKqub%d'dwfxfyf(d'gzfAfgowczkCkBfCfLiMixc,g-g)d*d.gDkDfEfFfGf:cHfEkIfJfyc;c=c?c+dzcAcvbBcCcDcroEcFkIkvoKfLfNiXt4 8b9bFc@c[c]c^c[ _c`c,dMfNf-dOfPfyoGcJkKk/g:gLkNqOiPiQizoQfRfRiOqSiTiAoHcMkPkSfTfUiVi;gwb=g[gZi{c|cUfGo}c?b.d/d0t1tIoRkIcSkVkMoVfWf2iTqUq2t3tPoWkJcXk0kToXfYf3iWqWo1kKc2k5k0oZf0f4iYq3o6kLc7k!k7o1f2f5i0q!o#kMc$k(k'o3f4f6i2q*o)kNc*k-k.o5f6f7i4q;o.kOc/k=k[o7f8f8i!t#t_o?kPc@k^k9f!f9i%t't8P9P)t!P#P$P*t+t|i,t-t.t/t:t;t=t?t@t[t]t%P!u.O^t_t`t{t|t}t~taubucudueufuguhuiujukulumunuoupuqurusutuuuvuwuxuyuzuAuBuCuDuEuFuGuHu#f$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}fip
57cdef CUresult cuDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, CUdevice dev, int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
58 return _driver._cuDeviceGetNvSciSyncAttributes(nvSciSyncAttrList, dev, flags)
61cdef CUresult cuDeviceSetMemPool(CUdevice dev, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
62 return _driver._cuDeviceSetMemPool(dev, pool) 2'P
65cdef CUresult cuDeviceGetMemPool(CUmemoryPool* pool, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
66 return _driver._cuDeviceGetMemPool(pool, dev) 2K N +b,b-bx 9 y z C { D w ^g_gHbV W kglg+i,i$zFC-iCdM KjPjQjOe' PeEd1c2c3c[hFdGdHdQeWbWjXb4cAg]hIdJdXj{hciXg}jbf( cf1d^d,c2dxi3d4d5ddf4bek5b-cyizi6d7dfkkkFi;gRkWk1k6k#k)k.k?k#f$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}fip
69cdef CUresult cuDeviceGetDefaultMemPool(CUmemoryPool* pool_out, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
70 return _driver._cuDeviceGetDefaultMemPool(pool_out, dev) 2'P
73cdef CUresult cuDeviceGetExecAffinitySupport(int* pi, CUexecAffinityType type, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
74 return _driver._cuDeviceGetExecAffinitySupport(pi, type, dev)
77cdef CUresult cuFlushGPUDirectRDMAWrites(CUflushGPUDirectRDMAWritesTarget target, CUflushGPUDirectRDMAWritesScope scope) except ?CUDA_ERROR_NOT_FOUND nogil:
78 return _driver._cuFlushGPUDirectRDMAWrites(target, scope)
81cdef CUresult cuDeviceGetProperties(CUdevprop* prop, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
82 return _driver._cuDeviceGetProperties(prop, dev)
85cdef CUresult cuDeviceComputeCapability(int* major, int* minor, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
86 return _driver._cuDeviceComputeCapability(major, minor, dev)
89cdef CUresult cuDevicePrimaryCtxRetain(CUcontext* pctx, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
90 return _driver._cuDevicePrimaryCtxRetain(pctx, dev) 2@r[r]r^r_r`r{r^p|r}r~rasbscsdsesfsgshsisjskslsmsnsospsqsar
93cdef CUresult cuDevicePrimaryCtxRelease(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
94 return _driver._cuDevicePrimaryCtxRelease_v2(dev) 2CZDZEZFZGZHZIZ^pJZKZLZMZNZOZPZQZRZSZTZUZVZWZXZYZZZ0Z1Z2Z3Z
97cdef CUresult cuDevicePrimaryCtxSetFlags(CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
98 return _driver._cuDevicePrimaryCtxSetFlags_v2(dev, flags)
101cdef CUresult cuDevicePrimaryCtxGetState(CUdevice dev, unsigned int* flags, int* active) except ?CUDA_ERROR_NOT_FOUND nogil:
102 return _driver._cuDevicePrimaryCtxGetState(dev, flags, active)
105cdef CUresult cuDevicePrimaryCtxReset(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
106 return _driver._cuDevicePrimaryCtxReset_v2(dev)
109cdef CUresult cuCtxCreate(CUcontext* pctx, CUctxCreateParams* ctxCreateParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
110 return _driver._cuCtxCreate_v4(pctx, ctxCreateParams, flags, dev) 2lymynyoypyqyrysytyuyvywyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMyNyOyPyQyRySyTyUyVyWy
113cdef CUresult cuCtxDestroy(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
114 return _driver._cuCtxDestroy_v2(ctx) 24Z5Z6Z7Z8Z9Z!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~Za0b0c0d0
117cdef CUresult cuCtxPushCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
118 return _driver._cuCtxPushCurrent_v2(ctx) 2GC(P
121cdef CUresult cuCtxPopCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
122 return _driver._cuCtxPopCurrent_v2(pctx) 2)P*P+P,P-P.P/P:P;P=P?P@P[P]P^P_P`P{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQHCICJCKCLCMCNCOCPCQCRCSCTCUCVCWCXCYCZC0C1CnQ2C3C4C5C6C#u7C8CoQpQ9C!C#C$C%C'C(C)C*C+C,C-C.CqQ/C:C;C=C?C@C[C]C^C_C`C{C|C}CrQ$u%u~CaDsQbDcDdDeDfDgDhDiDjDkDlDmDnDtQ'u(uoDpDuQqDrDsDtDuDvDwDxDyDzDADBDCDDDEDFDGDHDIDJDKDLDMDNDODPDQD)u*uRDSDTDUDVDWDXDYDZD0D1D2D3D4D5D6D7D+u,u8D9D!D#D$D%D'D(D)D*D+D,D-D.D/D:D;D-u.u=D?D@D[D]D^D_D`D{D|D}D~DaEbEcEdEeE/u:ufEgEhEiEjEkElEmEnEoEpEqErEsEtEuEvEwExEyEzEAEBECEDEvQEEFEGEHEIEJEwQxQyQzQAQBQCQDQEQFQGQHQIQJQKQLQMQNQOQPQQQRQSQTQUQVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Q,Q-Q.Q/Q:Q;Q=Q?Q@Q[Q]Q^Q_Q`Q{Q|Q}Q~QaRbRcRdReRfRgRhRiRjRKELEMENEkRlROEPEmRQERESETEnRUEVEoRpRqRrRsRtRuRvRwRxRyRzRARBRCRDRERFRGRHRIRJRKRLRMRNRORPRQRRRSRTRURVRWRXRYRZR0R1R2R3R4R5R6R7R8R9R!RWEXEYE#R$RGCZE0E1E%R2E(P3E4E'R(R)R*R+R,R-R.R/R:R;R=R?R@R[R]R^R_R`R{R|R}R~RaSbScSdSeSfSgShSiSjSkSlSmSnSoSpSqSrSsStSuSvSwSxSySzSASBSCSDSESFSGSHSISJSKSLSMSNSOSPSQSRSSSTSUSVSWSXSYSZS0S1S2S3S4S5S6S7S8S9S!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~SaTbTcTdTeTfTgThTiTjTkTlTmTnToTpTqTrTsTtTuTvTwTxTyTzTATBTCTDTETFTGTHTITJTKTLTMTNTOTPTQTRTSTTTUTVTWTXTYTZT0T1T2T3T4T5T6T7T8T9T!T#T$T%T'T(T)T*T+T,T-T.T/T:T;T=T?T@T[T]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHU5E6E7E8EIUJU9E!E;u=u#E$E%E'E(EKU)E*E+ELU,E-E.E/E:EMU;E=E?E@E[ENUOU]E^E?u@u_E`E{E|E}EPU~EaFbFQUcFdFeFfFgF[u]uhFiFjFkFlFmFnFoFpF^u_u`u{ubrcr|u}u~uavbvqFcvrFdvevsFfvgvhvivjvtFuFvFwFxFyFzFAFkvlvBFCFDFEFFFGFHFIFJFKFLFMFNFOFPFmvnvQFRFSFTFUFRUVFSUWFXFTUYFZF0F1F2F3F4FUU5F6Fovpv7F8F9F!F#FVU$FWU%F'FXU(F)F*F+F,F-Fqvrv.F/F:F;F=F?F@F[F]Fsvtvuvvv^FwvxvyvzvAvBvCvDv_FEv`FFvGv{FHvIvJvKvLvMvNvOvPvQvRvSvTvUv|FVvWv}F~FaGbGcGdGeGfGgGhGiGXvYvjGkGlGmGnGoGpGqGrGsGtGuGvGwGxGyGzGAGBGCGDGEGFGZv0vGGHGIGJGKGLGMGNGOGPGQGRG1v2vSGTGUGVGWGXGYGZG0G1G2G3G3v4v4G5G6G7G8GYU9G!G#GZU$G%G'G(G5v6v)G*G+G,G-G.G7v8v/G:G;G=G?G@G[G]G^G_G9v!v`G{G|G}G~G0UaHbHcHdHeHfHgHhHiH#v$vjHkHlHmHnHoHpHqHrH%v'v(v)vsH*v+vdrer,v-v.v/v:vtH;vuH=v?vvH@v[v]vwHxHyHzHAH1U2UBHCH^v_vDHEHFHGHHH3UIHJHKH4ULHMHNHOHPH`v{vQHRHSHTHUHVHWHXHYH|v}v~vawfrgrbwcwdwewfwZHgw0Hhwiw1Hjwkwlwmwnw2H3H4H5H6H7H8H9Howpw!H#H$H%H'H(H)H*H+H,H-H.H/H:H;Hqwrw=H?H@H[H]H5U^H6U_H`H7U{H|H}H~HaIbIcI8UdIeIswtwfIgIhIiIjI9UkI!UlImI#UnIoIpIqIrIsIuwvwtIuIvIwIxIyIzIAIBIwwxwywzwCIAwBwCwDwEwFwGwHwDIIwEIJwKwFILwMwNwOwPwQwRwSwTwUwVwWwXwYwGIZw0wHIIIJIKILIMINIOIPIQIRI1w2wSITIUIVIWIXIYIZI0I1I2I3I4I5I6I7I8I9I!I#I$I%I'I3w4w(I)I*I+I,I-I.I/I:I;I=I?I5w6w@I[I]I^I_I`I{I|I}I~IaJbJ7w8wcJdJeJfJgJ$UhJiJjJ%UkJlJmJnJ9w!woJpJqJrJsJtJ#w$wuJvJwJxJyJzJAJBJCJDJ%w'wEJFJGJHJIJ'UJJKJLJMJNJOJPJQJRJ(w)wSJTJUJVJWJXJYJZJ0J*w+w,w-w1J.w/whrir:w;w=w?w@w2J[w3J]w^w4J_w`w{w5J(U)U*U+U6J7J8J9J,U-U!J#J|w}w$J%J'J(J)J.U*J+J,J/U:U;U=U?U@U-J.J/J:J;J=J?J@J[U]U[J]J~wax^J_J`J{J|J^U}J~JaK_UbKcKdKeKfKgKhKiK`U{UjKkKbxcxlKmKnKoKpK|UqKrKsK}UtKuKvKwKxKyKzKAK~UaVBKCKdxexDKEKFKGKHKbVIKJKKKcVLKMKNKOKPKQKRKSKdVeVTKUKfxgxVKWKXKYKZKfV0K1K2KgV3K4K5K6K7K8K9K!KhViV#K$Khxix%K'K(K)K*KjV+K,K-KkV.K/K:K;K=K?K@K[KlVmV]K^Kjxkx_K`K{K|K}KnV~KaLbLoVpVcLdLeLfLgLhLiLjLqVrVkLlLlxmxmLnLoLpLqLsVrLsLtLtVuVuLvLwLxLvVwVxVyVzVAVBVCVDVEVFVGVHVIVJVKVLVMVNVOVPVQVRVSVTVUVVVWVXVYVZV0V1V2V3V4V5V6V7V8V9V!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~VaWbWcWdWeWfWgWhWiWjWkWlWmWnWoWpWqWrWsWtWuWvWwWxWyWzWAWBWCWDWEWFWGWHWIWJWKWLWMWNWOWPWQWRWSWTWUWVWWWXWYWZW0W1W2W3W4W5W6W7W8W9W!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~WaXbXcXdXeXfXgXhXiXjXkXlXmXnXoXpXqXrXsXtXuXvXwXxXyXzXAXBXCXDXEXFXGXHXIXJXKXLXMXNXOXPXQXRX
125cdef CUresult cuCtxSetCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
126 return _driver._cuCtxSetCurrent(ctx) 2cMdMeMfMgMhMiMjMkMlMmMnMoMpMqMrMsMtMuMvMwMxMyMzMAMBMCMe0DMEMFMGMHMIMXyYyZy0y1y2y3y4y5yEl}iFl6y~iGlHl7y8y9y!y#yJM$y%y'y(y)y*y+y,y-y.y/y:y;y=y?ySX@y[y]y^y_y`y{y|y}y~yazbzczdzezfzgzhzizIlJl@baj{d|dbjKlLlMlNlod}dIhJhKhLhOlPlQlRl[bcj~daedjSlTlUlVlpdbeMhNhOhPhWlXlYlejZljzfj0l1l2lgj3lhj4l5l6l7l]bijcedejj8l9l!l#lqdeeQhRhShTh$l%l'l(l^bkjfegelj)l*l+l,lrdheUhVhWhXh-l.l/l:l_bmjiejenj;l=l?l@lsdkeYhZh0h1h[l]l^l_l`bojlemepj`l{l|l}ltdne2h3h4h5h~lambmqjcmrjdmemfmsjgmtjhmimKMjmujkmvjlmmmLMMMNMOMPMQMRMSMTMUMVMWMXMYMZM0M1Mf02M3M4M5M6M7M8M9M!M#M$M%M'M(M)M*Mg0+M,M-M.M/M:M;M=M?M@M[M]M^M_M`M{M|M}M~Mh0aNbNcNdNeNfNgNhNiNi0j0k0l0m0n0o0kzp0q0r0s0t0u0v0w0x0y0z0A0B0C0D0E0F0jNkNlNmNnNoNpNG0qN_p`prN{p|p~paqbq-qsNomwjtspmxjqmyjuscqdqOueqfqgqhqiqjq/itNyLnxzLoxALpxBLzjCL.qH0vsI0J0K0L0M0N0O0P0Q0gg8qhg/qDLqxELFLGLHLILJLKLLLMLNLOLPLrxsxtxuxvxwxxxgpyxzxAxBxQLCxrm:qRLDxSLExab9qbb;qR0S0TLFxULGxVLAjT0U0V0wsW0X0wNxNyNzNANBNY0@r[r]r^r_r`r{r^p|r}r~rasbscsdsesfsgshsisjskslsmsnsospsqs^g_gZ00010203040CNDN5060VPWL7080Tc0 UcENsmFN90!0#0$0GNHNIN%0JNKNLNMNNNONPN`gjp{g|gkp}g~gahjgbhchdhalTzBjCjtetmumDjEjFjQNGjHjIjUzVzWzXzYzZz0z1z2z3z4z5z6z7z8z9z!z#zRNIb:iue]d'0(0SN)0ehfhghhhihVcjhkhlhmhnhWcohphqhrhXcshthuhvhwhxhyhzhAhBhYcChDhMsNsOsPsQsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s%s's(s)s*s+s`B,s-sbl_d{bHxTXjrkrIxkglgJxKxLxMxoqpqUXVX.sWX/sXXYXZX:s0X1X;s=s2X?s3X4X5X6X@s7X[s]s8X9X!X#X$X%X^s'X(X_s`s{sXL)X|s*X+X,X-X}s.X/X:X;X~s=X?X@Xat[X]Xbtctdt^Xet_Xftgt`X{X|X}Xhtit~XjtktaYbYcYltdYmteYntfYgYhYotiYptjYkYlYqtmYnYoYrtstpYttutvtqYcl+i,i%zTb*0'z3P+0,0{k|bPu-0|kTNQu.07hUN8h/09hVNRuWNib:0-i;0ud=0}k?0!hXNveYNvd@0}b[0#h]0weZN$h^0xe_0%h`0ye{0'h|0ze}0wd~0~ba1(hb1mgc1ngd1e1Zc0Nf1ogg11Npgh1i1qgj12Nrgk13Nxdl1m1sgn1o1)h4NAe5Nyd6Nacp1*hq1Be7N+hr1Ces1,h8NDe9N-ht1Ee!Nzd#Nbcu1.hv1Few1tgx1ug$N/hy1Ad%N0c'NBdz14PxtvmcclpCd.i~kA1UbB1dcGe(NC1D1E1F1G1edfd} )Ngdqq*Nxmym+Nzm,NAmBmCm-NDm.N/N:N;N=N?N@N[N]N^NEmFmGmHmytztAtBtCtDtEtFtGtImJmKmLmMmNmOmPmQmRmSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!m#m$m%m'm(m)m*m+m,m-m.m/m:m;m=m?m@m[m]m^m_m`m{m|mNx}mOx~manbncndnenfngnhninOAjnH1knI1;iJ1lnK1mnKjecrq_N`NLj)zMjNjOj*znnonpnqnHeIe=hsq+zHtrnsnPjtnItunQjfctq{N,zRj-zSjTjUj.zvnwnxnynJeKe?huq/zJtznAnVbLeMeVjvgwgxgDdNe@hygzgOe' PeEd1c2c3c[hFdGdHdQeWbWjXb4cAg]hIdJdjbkbYb, - . / ^hlbBgCgDgEg_hBnCn5cKdFgvqlrDnEnXjgcwqYjZj0j1j:zFnGnHnInRe|NSe`hxq;zJnKn2j{hZbLn=z|hKt}h~haiLt3j4j5j6jLd?zMdGgMnMtyq7j8j9jmbNdOdbiTeUeVe6cWeHgXeYemrci0bNn@zdi!j#jeiNt$j%j'j(jPd[zQdIgOnOt)j*jfigiZe0e1e2ehi3e4e5e6enbRdSd7e8e9eTdJg!e#ePnhczq+j,j-j.jQnRnSn$e%eii]zTnUnKgLgMgNgVnWnXnYnZnjiicOgPgUdVdQg/j'e(e)e*e7c+e:j,e-ejc8c9c!cWdkclcobmcncoc0npcAq;j=j?j@j^z1n2n3n4n.e/ekiBq_z5n6n3 1b2bqc#c$c%c'c: (c)cXd:e;eYd=e?e[jrclimi@e[eni7nRgSgTg8n]eZdUg9nVgWg!nsc]j^j_j`j#n$n%n^e_eoi'n(npiXgpb{jPtYgCqZg0g1gDqdlqirisi*cQt+c`e|jEqtiui)n*n}jtcFq}N~N~j`zakbkck{z+n,n-n.n{e|eviGq|zRt/n:n3b}e~edk2g3g4g0dafwi5g6gbf( cf1d^d,c2dxi3d4d5ddf4bek5b-cyizi6d7dqbrb6b; = ? @ Aisb7g8g9g!gBi;n=n.c8d#gHq?n@n[nfkucIqgkhkikjk}z]n^n_n`nefaOffCiSt~z{n|n}nkkvcJqbOlkaAmknkokbA~naobocogfcOhfDiTtcAUtdoeopktb9d!dEiifjfkf/clf$gmfnfqkFi7bfodAGirkskHiVttkukvkwk#deA$d%gKqWtxkykIiJiofpfqfrfKisftfufvfub%d'dwfxfyf(d'gzfAfgowcLqzkAkBkCkhoiojoBfCfLifAkolo(g)g*g+gmonooopoqoMixc,g-g)d*d.gDkDfEfFfGf:cHfEkIfJfyc;c=c?c+dzcAcvbBcCcDcroEcMqFkGkHkIkgAsotouovoKfLfNiXthAwoxo4 8b9bFc@c[c]c^c[ _c`c,dMfNf-dOfPfyoGcJkKk/g:gLkNqOiPiQizoQfRfRiOqSiTiAoHcMkNkOkPkBoCoDoSfTfUiEoFoVi;gwbQkYt=gPq?g@g[gQqWiXiYiZi{cZt|cUfGoRq0i1iHodOeO}c?b.d/d0t1tIoRkIcSqfOiASkjATkUkVkkAJoKoLoMoVfWf2iTqUqgO2t3thOlA4tNoOoPoWkJcVqiOjOXkmAYkZk0knAQoRoSoToXfYf3iWqoA5tUoVoWo1kKcXqkOpA2kqA3k4k5krAXoYoZo0oZf0f4iYqsA6t1o2o3o6kLcZqlOtA7kuA8k9k!kvA4o5o6o7o1f2f5i0qwA7t8o9o!o#kMc1qmOxA$kyA%k'k(kzA#o$o%o'o3f4f6i2qAA8t(o)o*o)kNc3qnOBA*kCA+k,k-kDA+o,o-o.o5f6f7i4qEA9t/o:o;o.kOc5qoOpO/kFA:k;k=kGA=o?o@o[o7f8f8i!t#tHA$t]o^o_o?kPc6qqOrO@kIA[k]k^kJA`o{o|oar9f!f9i%t'tKA(t}o~osOtOL1uOM1vON1wOxOyOO1P1zOAOBOCODOEOFOQ1GOHOIOJOKOLOR1MONOOOS1POQOROSOTOT1UOVOWOXOYOZO0O1O2O3O4O5O6OU17OV18O9O!OW1X1#OY1Z1$O%O'O01(O)O*O+O11,O-OrY/O:O;O=O?O@O[O]O^O_O`O{O|O}O~OaPbPcPdPePnrfPgPhPiPjP^t_t`t{t|t}t~taubucudueufuguhuiujukulumunuoupuqurusutuuuvuwuxuyuzuAuBuCuDuEukPlPmPFuGuHu21nPoPpP31415161718191qPrPsPtP!1#1$1%1'1uPvPwPxPyP#f$forpr%f'f(f)f*fqr+f,f-frr.fsr/ftr:f;fur=fvr?fwr@fxr[fyrzr]f^f_f`f{fAr|fBr}f(1zP)1*1AP+1,1-1BPCP.1/1DPEP:1FPGPHPIPJP;1KP=1LPMPNPOPPPQPRP?1SPTP@1UP
129cdef CUresult cuCtxGetCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
130 return _driver._cuCtxGetCurrent(pctx) 2a rs)P*P+P,P-P.P/P:P;P=P?P@P[P]P^P_P`P{P|P}P~PaQbQcQdQeQfQgQhQiQjQkQlQmQHCICJCKCLCPxMCNCOCPCQCRCSCTCUCVCWCXCYCZC0C1CnQ2C3C4C5C6C#u7C8CoQpQ9C!C#C$C%C6 'C7 (C8 )C* *C#b+C$b,C%b-CQc.CqQ/C:C;C=C?C@C[C]C^C_C`C{C|C}CrQ$u%u~CaDsQMlbDNlcDdD}deDIhfDJhgDKhhDLhiDOljDPlkDlDmDnDtQ'u(uoDpDuQUlqDVlrDsDbetDMhuDNhvDOhwDPhxDWlyDXlzDADBDCDDDEDFDGDHDIDJDKDLDMDNDODPDQD)u*uRDSDTD!lUD#lVDWDeeXDQhYDRhZDSh0DTh1D$l2D%l3D4D5D6D7D+u,u8D9D!D+l#D,l$D%Dhe'DUh(DVh)DWh*DXh+D-l,D.l-D.D/D:D;D-u.u=D?D@D?l[D@l]D^Dke_DYh`DZh{D0h|D1h}D[l~D]laEbEcEdEeE/u:ufEgEhE|liE}ljEkEnelE2hmE3hnE4hoE5hpE~lqEamrEsEtEuEvEwExEyEzEAEBECEDEvQEEFEGEHEIEJEAlwQxQyQzQAQQxBQCQDQEQFQGQHQIQJQBlKQLQMQNQOQPQQQRQSQmpTQnpUQopVQppWQCbXQDbYQEbZQFb0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Q,Q=i-Q.Q/Q:Q;Q=Q?Q@Q[Q]Qb ^Q_Q=b`Q{Q|Q}Q~QaRbRcRdReRfRgRhRiRjRKELEMENEkRlROEPEmRQERESETEnRUEVEoRpRqRrRsRtRuRvRwRxRyRzRARBRCRSATA^gDR_gERFRGRHRIRJRKRLRMRNRORsYxsUAVAWAXAYAZA0A1A2AtYys3A4Azs5A6A7A8A9A!A#A$A%AAs'A(A)A*A+A,A-A.A/ABs:A;A=A?A@A[A]A^A_ACs`A{A|A}A~AaBbBDscBdBeBfBgBhBiBjBkBlBmBnBEsoBpBFsqBrBsBtBuBvBwBxByBzBABBBCBGsDBEBFBHsGBHBIBJBKBIsLBMBNBOBPBQBRBSBTBUBVBWBXBYBZB0B1B2B3B4B5B6B7B8B9B!B#B$BJs%B'B(BKs)BLs*B+B,B-B.B/B:B;B=B?B@B[B]B^B_BPRWLQRRRSRLAuYMA[1NATc0 UcTRsmURVRWRXRYRZR0R1R2R3R4R5R6R7R8R9Rel!RWEXEYEV #RW $RGCZE0E1E%R2E3E4E'R(R)R*R+R,R-R.R/R:R;R=R?R@R[R]R^R_R`Rue{R|R}R~RVcWcXcYcaSbScSdSeSfSgShSiSjSkSlSmSnSoSpSqSrSsStSuSvSwSxSySzSASBSCSDSESFSGSHSISJS{b.s/s:s;s=s?s@s[s]s^s_s`s{sXL|s}s~satbtctdtetftgthtitjtktltmtntotptqtrtstttutvtKSLSMS|bNSOSPSQSRSSSTSUSVSWSXS(zYSZS0S1S2S3S4S5S6S7S8S9S!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~SaTbTcTdTeTfTgThTiTjTkTlTmTnToTxtvmccCdpTqTrTsTtTuTvTwT} xTqqyTzTATBTCTDTETFTGTHTITHhJTKTLTMTNTOTPTQTRTSTTTUTVTWTXTYTZT0T1T2T3T4T5T6T7T8T9T!T#T$T%T'T(T)T*T+T,T-T.T/T:T;T=T?T@T[T]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHU5E6E7Erq8EIUJU9E!E;u=u#E$E%Eon'Epn(EKU)EIe*E=h+ELU,E-Ern.Esn/E:EMU;E=E?E@Etq[ENUOU]E^E?u@u_E`E{Ewn|Exn}EPU~EKeaF?hbFQUcFdFzneFAnfFgF[u]uhFiFwgjFxgkFlFNemF@hnFygoFzgpF^u_uPe`u{ubrcr|u}u~uGdavHdbvqFcvrFXbdv4cevsFfvIdgvJdhvivjvtF, uF- vF. wF/ xF^hyFlbzFBgAFCgkvDglvEgBF_hCFBnDFCnEF5cFFKdGFFgHFvqIFlrJFDnKFLFMFNFwqOFPFmvnvQFRFSFGnTFHnUFRUVFSUSeWF`hXFTUYFJnZFKn0F1F2F3FLn4FUU5F6Fovpv7F8F9F4j!F5j#FVU$FWUMd%FGg'FXU(F)F7j*F8j+F,F-Fqvrv.F/FUe:FVe;F=FWe?FHg@FXe[FYe]FsvtvuvNnvv^FwvxvyvzvAvBv%jCv'jDv_FEv`FQdFvIgGv{FHv)jIv*jJvKvLvZeMv0eNv1eOv2ePvQv3eRv4eSv5eTv6eUv|FVvWv}F8e~F9eaGTdbGJgcG!edG#eeGfGgGzqhGiGXvYvjGkGRnlGSnmGnG%eoGiipGqGTnrGUnsGKgtGLguGMgvGNgwGVnxGWnyGXnzGYnAGZnBGCGDGOgEGFGZv0vGGHGIG(eJG)eKGLG7cMG+eNGOG,ePG-eQGRG1v2vSGTGkcUGlcVGobWGmcXGncYGocZG0G1GAq2G3G3v4v4G5G6G2n7G3n8GYU9G/e!Gki#GZU$G5n%G6n'G3 (G1b5v2b6vqc)G#c*G$c+G%c,G'c-G: .G(c7v)c8vXd/G:e:G;e;GYd=G=e?G?e@G[G]Gli^G_G9v!v`G{G|GSg}GTg~G0UaHZdbHUgcHdHVgeHWgfHgHhHiH#v$vjHkH$nlH%nmHnH_eoHoipH'nqH(nrH%v'v(v{j)vsH*v+vdrer,v-v.vqi/vri:vtH;vuH+c=v`e?vvH@vti[vui]v)nwHxHyHzHFqAH1U2UBHCH^v_vDHEHFH,nGH-nHH3UIH|eJHviKH4ULHMH/nNH:nOHPH`v{vQHRH3gSH4gTHUHafVHwiWH5gXH6gYH|v}vcf~vawfrgrbwcwdw4dew5dfwZHgw0H5bhw-ciw1Hjw6dkw7dlwmwnw2H; 3H= 4H? 5H@ 6HAi7Hsb8H7g9H8gow9gpw!g!HBi#H;n$H=n%H.c'H8d(H#g)HHq*H?n+H@n,H-H.H/HIq:H;Hqwrw=H?H@H^n[H_n]H5U^H6Uff_HCi`H7U{H{n|H|n}H~HaIbIJqcI8UdIeIswtwfIgIhIaoiIbojI9UkI!UhflIDimI#UnIoIdopIeoqIrIsIuwvwtIuIjfvIkfwIxIlfyI$gzImfAInfBIwwxwywfozwCIAwBwCwDwEwFwukGwvkHwDIIwEI$dJw%gKwFILwxkMwykNwOwPwofQwpfRwqfSwrfTwUwsfVwtfWwufXwvfYwGIZw0wHIxfIIyfJI(dKI'gLIzfMIAfNIOIPILqQIRI1w2wSITIioUIjoVIWICfXILiYIZIko0Ilo1I(g2I)g3I*g4I+g5Imo6Ino7Ioo8Ipo9Iqo!I#I$I,g%I'I3w4w(I)I*IEf+IFf,I-I:c.IHf/I:IIf;IJf=I?I5w6w@I[Izc]IAc^Ivb_IBc`ICc{IDc|I}I~IMqaJbJ7w8wcJdJeJtofJuogJ$UhJLfiJNijJ%UkJwolJxomJ4 nJ8b9w9b!wFcoJ@cpJ[cqJ]crJ^csJ[ tJ_c#w`c$w,duJMfvJNfwJ-dxJOfyJPfzJAJBJJkCJDJ%w'wEJFJGJPiHJQiIJ'UJJRfKJRiLJMJSiNJTiOJPJQJRJ(w)wSJTJCoUJDoVJWJTfXJUiYJEoZJFo0J*w+w,wQk-w1J.w/whrir:w;w=wXi?wYi@w2J[w3J|c]wUf^w4J_w0i`w1i{wHo5J(U)U*U+U6J7J8JSq9J,U-U!J#J|w}w$J%J'JKo(JLo)J.U*JWf+J2i,J/U:U;U=U?U@U-J.JNo/JOo:J;J=J?JVq@J[U]U[J]J~wax^J_J`JRo{JSo|J^U}JYf~J3iaK_UbKcKUodKVoeKfKgKhKXqiK`U{UjKkKbxcxlKmKnKYooKZopK|UqK0frK4isK}UtKuK1ovK2owKxKyKzKZqAK~UaVBKCKdxexDKEKFK5oGK6oHKbVIK2fJK5iKKcVLKMK8oNK9oOKPKQKRK1qSKdVeVTKUKfxgxVKWKXK$oYK%oZKfV0K4f1K6i2KgV3K4K(o5K)o6K7K8K9K3q!KhViV#K$Khxix%K'K(K,o)K-o*KjV+K6f,K7i-KkV.K/K/o:K:o;K=K?K@K5q[KlVmV]K^Kjxkx_K`K{K?o|K@o}KnV~K8faL8ibLoVpVcLdL]oeL^ofLgLhLiL6qjLqVrVkLlLlxmxmLnLoL{opL|oqLsVrL!fsL9itLtVuVuLvL}owL~oxLvVwV)txVyVzVAVBVCVDVEVFVGVHVIVJVKVLVMVNVOVPVQVRVSVTVUVVVWVXVYVZV0V1V2V3V4V5V6V7V8V9V!V#V*tvY+t|i$V%V'V(V)V*V+V,V-V.V/V:V;V=V,t-t.t/t:t;t?V=t?t@t[twY]t@V[V]V^V_V`V{V|V}V~VaWbWcWdWeWfWgWhWiWjWkWlWCrmWnWoWpWqWrWsWtWuWvWwWxWyWzWAWBWCWDWEWFWGWHWIWJWKWLWMWNWOWPWQWRWSWTWUWVWWWXWYWZW0W1W2W3W4W5W6W7W8W9W!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~WaXbXcXdXeXfXgXhXiX#f$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}fjXkXlXmXnXoXpXqXrXsXtXuXvXwXxXyXzXAXBXCXDXEXFXGXHXIXJXKXLXMXNXOXPXQXRX
133cdef CUresult cuCtxGetDevice(CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil:
134 return _driver._cuCtxGetDevice(device) 2a rsJbKbcgS T ?i5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J PAQA!q]1;rMuRANuEl}iFl~iGlHl#qhd~cadbd:d2 .bidjdybzbAb!bBb6 7 8 * #b$b%bQc$q%q'q(q)q*q$i_kIlJl@baj{d|dbjod}dIhJhKhLhQlRl[bcj~daedjpdbeMhNhOhPhYlejZlfj0l1l2lgj3lhj4l5l6l7l]bijcedejjqdeeQhRhShTh'l(l^bkjfegeljrdheUhVhWhXh/l:l_bmjiejenjsdkeYhZh0h1h^l_l`bojlemepjtdne2h3h4h5hbmqjcmrjdmemfmsjgmtjhmimjmujkmvjlmmm`k+q;dcdWPXPYPZP0P1PCbDbEbFb/b:b'b~ =d@iLbMb?d[iK N ,qagX ^ _ (b;bO L A F B b x 9 y z C { D w P Q R ^1E Y Z Gb)b*bddScU _p`p_1{p|p~paqbq-qomwjtspmxjDrqmEryjuscqdqOueqfqgqhqiqjq/inxoxpxzj.q/qqxrxsxtxuxvxwxxxgpyxzxAxBxCx:qDxEx;qFxGxAjRxSxTxUxVxWxSATA^g_gYLXxsYxsUAVAWAXAYAZA0A1A2AtYys3A4Azs5A6A7A8A9A!A#A$A%AAs'A(A)A*A+A,A-A.A/ABs:A;A=A?A@A[A]A^A_ACs`A{A|A}A~AaBbBDscBdBeBfBgBhBiBjBkBlBmBnBEsoBpBFsqBrBsBtBuBvBwBxByBzBABBBCBGsDBEBFBHsGBHBIBJBKBIsLBMBNBOBPBQBRBSBTBUBVBWBXBYBZB0B1B2B3B4B5B6B7B8B9B!B#B$BJs%B'B(BKs)BLs*B+B,B-B.B/B:B;B=B?B@B[B]B^B_BWLLAuYMANATc0 UcZLsm0Lflglhliljlkl` llmlnlolpl]iEhRcIb:iue]d`12P^iehfhghhhihVcjhkhlhmhnhWcohphqhrhXcshthuhvhwhxhyhzhAhBhYcChDh{1MsNsOs|1PsQsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s8s9s!s#s$s%s's(s)s*s+s`B,s-sbl_d{bHxTXjrkrIxUXVX.sWX/sXXYXZX:s0X1X;s=s2X?s3X4X5X6X@s7X[s]s8X9X!X#X$X%X^s'X(X_s`s{sXL)X|s*X+X,X-X}s.X/X:X;X~s=X?X@Xat[X]Xbtctdt^Xet_Xftgt`X{X|X}Xhtit~XjtktaYbYcYltdYmteYntfYgYhYotiYptjYkYlYqtmYnYoYrtstpYttutvtqYcl+i,iTb}1{k|bPu|kQu7h8h9hRuib-iud}k(z!hvevd}b#hwe$hxe%hye'hzewd~b(hmgng{BZc|Bog}Bpg~BqgaCrgbCxdcCsgdC)hAeydac*hBe+hCe,hDe-hEezdbc.hFetgug/hAd0cBdxtvmcclpCd.i~kUbdcGewm:h;h5Pqlrledfd} 6Pgdqq7PxmxYym=qzm?qAmyYBmzYCmM DmHh@q[q]q^q_q`q{q|q}q~qEmFmGmHmytztAtBtCtDtEtFtGteCImfCJmgCKmhCLmiCMmjCNmSuOmTuPmUuQmVuRmWuSmXuTmYuUmZuVm0uWm1uXm2uYm3uZm4u0m5u1m6u2m7u3m8u4m9u5m~16ma27mkC8mlC9mmC!mnC#moC$mpC%mqC'mrC(msC)mtC*muC+mvC,mwC-mxC.myC/mzC:mAC;mBC=mCC?mDC@mEC[mb2]mAY^mBY_mCY`mDY{mEY|mFYNxGY}mHYOxIY~mJYanKYbnLYcnMYdnNYenOYfnPYgnhnmnecLjOjqnHeIe=hsqtnunfcRjUjynJeKe?huqVbLeMeVjvgwgxgDdNe@hygzgOe' Ed3cQeWbXb4cAgjbkbYb, - . / ^hlbBgEg5cKdFgEngcYj1jInReSe`hxq2jZb|hai6jLdMdGgMn9jmbNdOdbiTeUeVe6cWeHgXeYemr0bdiei(jPdQdIgOnnbRdSd7e8e9eTdJg!e#ePnhc+j.j$e%eiijiicOgPgUdVdQg/j'e(e)e*e7c+e:j,e-ejc8c9c!cWdkclcobmcncoc0npc;j@j4n.e/ekiBq3 1b2bqc#c$c%c'c: (c)cXd:e;eYd=e?e[jrclimi@e[eni7nRgSgTg8n]eZdUg9nVgWg!nsc]j`j^e_eoipipbYg1gsi*c+c`e|j*ntc~jck.n{e|eviGq3b}e~edk2g3g4g0dafwi5g6gbf( 1d2ddf4b5b-cyiqbrb6b; = ? @ Aisb7g!g.c8d#g[nucgkjk`nefffCiSt}nvclkokcogfhfDiTtpktb9d!dEiifjfkf/clf$gmfnfqk7bGiHiwk#d$d%gKqub%d'dwfxfyf(d'gzfAfgowczkCkBfCfLiMixc,g-g)d*d.gDkDfEfFfGf:cHfEkIfJfyc;c=c?c+dzcAcvbBcCcDcroEcFkIkvoKfLfNiXt4 8b9bFc@c[c]c^c[ _c`c,dMfNf-dOfPfyoGcJkKk/g:gLkNqOiPiQizoQfRfRiOqSiTiAoHcMkPkSfTfUiViwb=g[gZi{c|cUfGo0t1tIoIcSkVkMoVfWf2iTqUq2t3tPoJcXk0kToXfYf3iWqWoKc2k5k0oZf0f4iYq3oLc7k!k7o1f2f5i0q!oMc$k(k'o3f4f6i2q*oNc*k-k.o5f6f7i4q;oOc/k=k[o7f8f8i!t#t_oPc@k^kar9f!f9i%t't8P9P)tc2!P#P$P*tvY+t|i,t-t.t/t:t;td2=t?t@t[twY]t%P!urYe2YxZx0x1x2x3xCr4x5x6x7x8x9x!x#x$xsl%xnrFr'xFh(x^t_t`t{t|t}t~taubucudueufuguhuiujukulumunuoupuqurusutuuuvuwuxuyuzuAuBuCuDuEuFuGuHuf2g2h2i2j2k2l2m2n2o2p2q2r2s2t2u2v2w2x2y2z2A2B2C2#f$forpr%f'f(f)f*fqr+f,f-frr.fsr/ftr:f;fur=fvr?fwr@fxr[fyrzr]f^f_f`f{fAr|fBr}fD2E2
137cdef CUresult cuCtxGetFlags(unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
138 return _driver._cuCtxGetFlags(flags)
141cdef CUresult cuCtxSetFlags(unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
142 return _driver._cuCtxSetFlags(flags)
145cdef CUresult cuCtxGetId(CUcontext ctx, unsigned long long* ctxId) except ?CUDA_ERROR_NOT_FOUND nogil:
146 return _driver._cuCtxGetId(ctx, ctxId)
149cdef CUresult cuCtxSynchronize() except ?CUDA_ERROR_NOT_FOUND nogil:
150 return _driver._cuCtxSynchronize()
153cdef CUresult cuCtxSetLimit(CUlimit limit, size_t value) except ?CUDA_ERROR_NOT_FOUND nogil:
154 return _driver._cuCtxSetLimit(limit, value)
157cdef CUresult cuCtxGetLimit(size_t* pvalue, CUlimit limit) except ?CUDA_ERROR_NOT_FOUND nogil:
158 return _driver._cuCtxGetLimit(pvalue, limit)
161cdef CUresult cuCtxGetCacheConfig(CUfunc_cache* pconfig) except ?CUDA_ERROR_NOT_FOUND nogil:
162 return _driver._cuCtxGetCacheConfig(pconfig)
165cdef CUresult cuCtxSetCacheConfig(CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
166 return _driver._cuCtxSetCacheConfig(config)
169cdef CUresult cuCtxGetApiVersion(CUcontext ctx, unsigned int* version) except ?CUDA_ERROR_NOT_FOUND nogil:
170 return _driver._cuCtxGetApiVersion(ctx, version)
173cdef CUresult cuCtxGetStreamPriorityRange(int* leastPriority, int* greatestPriority) except ?CUDA_ERROR_NOT_FOUND nogil:
174 return _driver._cuCtxGetStreamPriorityRange(leastPriority, greatestPriority) 2JbKbcgS T ?i5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J hd~cadbd:d2 .bidjdybzbAb!bBb6 7 8 * #b$b%bQccd/b:bLbMbK N X ^ _ ;bO L A F B b +b,b-bkdldmdx 9 y z C { D w P Q R NbObPb! # $ E Y Z Gb)b*bddScU dg`dtlulndvlwlDrEregfgqprpsptpup/i% ] bp]g!i#icpdpepfpxl1L2LigQbabbb+ ~fRbSbcbdbebfbgbhbRxSxTxUxVxWxXxTc0 Ucflglhliljlkl` llmlnlolpl]iEhRc`gjp{g|gkp}g~gahjgbhchdhal)xHbV W QY3L_iIb:iue]d^i_d{bGrHrvpIrwpJrKrxpypLrMrNrzpOrApBpCpDpEpFpGpHpIpPrJpKpLpMpQrNpOpRrSrTrUrPpVrQpWrXrRpSpYrZr0rTp1rUpVpWpXpYpZp0p1p2p2r3p4p5p6p3r7p8p4r5r6r7r9p8r!p9r!r#p$p#r$r%r%p'r'p(p)p*p+p,p-p.p/p(r:p;p=p?p)r@p[p*r+rTbiblpUbqlrlM ;iHtItJtyqpiXgpb{jPtYgCqZg0g1gDqdlqirisi*cQt+c`e|jEqtiuiRtUtVi;gwbQkYt=gPq?g@g[gQqWiXiYiZi{cZt|cUfGoRq0i1i.d/d4t5t6t7t8t9t$t(tYxZx0x1x2x3xCr4x5x6x7x8x9x!x#x$xsl%xnrFr'xFh(x
177cdef CUresult cuCtxResetPersistingL2Cache() except ?CUDA_ERROR_NOT_FOUND nogil:
178 return _driver._cuCtxResetPersistingL2Cache()
181cdef CUresult cuCtxGetExecAffinity(CUexecAffinityParam* pExecAffinity, CUexecAffinityType type) except ?CUDA_ERROR_NOT_FOUND nogil:
182 return _driver._cuCtxGetExecAffinity(pExecAffinity, type)
185cdef CUresult cuCtxRecordEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
186 return _driver._cuCtxRecordEvent(hCtx, hEvent)
189cdef CUresult cuCtxWaitEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
190 return _driver._cuCtxWaitEvent(hCtx, hEvent)
193cdef CUresult cuCtxAttach(CUcontext* pctx, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
194 return _driver._cuCtxAttach(pctx, flags)
197cdef CUresult cuCtxDetach(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
198 return _driver._cuCtxDetach(ctx)
201cdef CUresult cuCtxGetSharedMemConfig(CUsharedconfig* pConfig) except ?CUDA_ERROR_NOT_FOUND nogil:
202 return _driver._cuCtxGetSharedMemConfig(pConfig)
205cdef CUresult cuCtxSetSharedMemConfig(CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
206 return _driver._cuCtxSetSharedMemConfig(config)
209cdef CUresult cuModuleLoad(CUmodule* module, const char* fname) except ?CUDA_ERROR_NOT_FOUND nogil:
210 return _driver._cuModuleLoad(module, fname)
213cdef CUresult cuModuleLoadData(CUmodule* module, const void* image) except ?CUDA_ERROR_NOT_FOUND nogil:
214 return _driver._cuModuleLoadData(module, image) 2@d[d%i'i(ibg)i*i
217cdef CUresult cuModuleLoadDataEx(CUmodule* module, const void* image, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
218 return _driver._cuModuleLoadDataEx(module, image, numOptions, options, optionValues) 2F2
221cdef CUresult cuModuleLoadFatBinary(CUmodule* module, const void* fatCubin) except ?CUDA_ERROR_NOT_FOUND nogil:
222 return _driver._cuModuleLoadFatBinary(module, fatCubin)
225cdef CUresult cuModuleUnload(CUmodule hmod) except ?CUDA_ERROR_NOT_FOUND nogil:
226 return _driver._cuModuleUnload(hmod) 2@d[d%i'i(ibg)i*i
229cdef CUresult cuModuleGetLoadingMode(CUmoduleLoadingMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
230 return _driver._cuModuleGetLoadingMode(mode)
233cdef CUresult cuModuleGetFunction(CUfunction* hfunc, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
234 return _driver._cuModuleGetFunction(hfunc, hmod, name) 2@d[d%i'i(ibg)i*i
237cdef CUresult cuModuleGetFunctionCount(unsigned int* count, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
238 return _driver._cuModuleGetFunctionCount(count, mod)
241cdef CUresult cuModuleEnumerateFunctions(CUfunction* functions, unsigned int numFunctions, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil:
242 return _driver._cuModuleEnumerateFunctions(functions, numFunctions, mod)
245cdef CUresult cuModuleGetGlobal(CUdeviceptr* dptr, size_t* bytes, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
246 return _driver._cuModuleGetGlobal_v2(dptr, bytes, hmod, name) 2bg
249cdef CUresult cuLinkCreate(unsigned int numOptions, CUjit_option* options, void** optionValues, CUlinkState* stateOut) except ?CUDA_ERROR_NOT_FOUND nogil:
250 return _driver._cuLinkCreate_v2(numOptions, options, optionValues, stateOut)
253cdef CUresult cuLinkAddData(CUlinkState state, CUjitInputType type, void* data, size_t size, const char* name, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
254 return _driver._cuLinkAddData_v2(state, type, data, size, name, numOptions, options, optionValues)
257cdef CUresult cuLinkAddFile(CUlinkState state, CUjitInputType type, const char* path, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil:
258 return _driver._cuLinkAddFile_v2(state, type, path, numOptions, options, optionValues)
261cdef CUresult cuLinkComplete(CUlinkState state, void** cubinOut, size_t* sizeOut) except ?CUDA_ERROR_NOT_FOUND nogil:
262 return _driver._cuLinkComplete(state, cubinOut, sizeOut)
265cdef CUresult cuLinkDestroy(CUlinkState state) except ?CUDA_ERROR_NOT_FOUND nogil:
266 return _driver._cuLinkDestroy(state)
269cdef CUresult cuModuleGetTexRef(CUtexref* pTexRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
270 return _driver._cuModuleGetTexRef(pTexRef, hmod, name)
273cdef CUresult cuModuleGetSurfRef(CUsurfref* pSurfRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
274 return _driver._cuModuleGetSurfRef(pSurfRef, hmod, name)
277cdef CUresult cuLibraryLoadData(CUlibrary* library, const void* code, CUjit_option* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, CUlibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?CUDA_ERROR_NOT_FOUND nogil:
278 return _driver._cuLibraryLoadData(library, code, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2S T 5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J 2 ybzbAb!bBb$i_k@bod[bpd]bqd^brd_bsd`btd;dCbDbEbFb'bK N ,qagX ^ _ (bO L A F B b x 9 y z C { D w P Q R E Y Z Gb)b*bddScU % ] 0 ` RctetmumIb]d^iehfhghhhihVcjhkhlhmhnhWcohphqhrhXcshthuhvhwhxhyhzhAhBhYcChDhxmym=qzm?qAmBmCmM DmHh@q[q]q^q_q`q{q|q}q~qEmFmGmRYHmSYG2ImJmKmLmMmNmOmPmQmRmSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!m#m$m%m'm(m)m*m+m,m-m.m/m:m;m=m?m@m[m]m^m_m`m{m|mNx}mOx~manbncndnenfngnhnecqnHesqtnfcynJeuqVbDd' QeWbAgjbkbYb, - . / lb5cgcInRexqZb6jLdMnmb6c0b(jPdOnnbhc$ejiicOgPgUdVdQg/j'e(e)e*e7c+e:j,e-ejc8c9c!cWdkclcobmcncocpc4n.eBq3 : [jrclimi@e[eni7nRgSgTg8n]eZdUg9nVgWgsc^epbsi*c|jtc.n{eGq3b0d( df4bqbrb6b; = ? @ sb.cuc`nefvccogftb/c7bwk#dubwcBfMixc,g-g)d*d.gDkDfEfFfGf:cHfEkIfJfyc;c=c?c+dzcAcvbBcCcDcEcvoKf4 [ GczoQfHcSfwbZi{cIcMoVfTqUqJcToXfWqKc0oZfYqLc7o1f0qMc'o3f2qNc.o5f4qOc[o7fPcar9f|i!u
281cdef CUresult cuLibraryLoadFromFile(CUlibrary* library, const char* fileName, CUjit_option* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, CUlibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?CUDA_ERROR_NOT_FOUND nogil:
282 return _driver._cuLibraryLoadFromFile(library, fileName, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2TYUYVYWY
285cdef CUresult cuLibraryUnload(CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
286 return _driver._cuLibraryUnload(library)
289cdef CUresult cuLibraryGetKernel(CUkernel* pKernel, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
290 return _driver._cuLibraryGetKernel(pKernel, library, name) 2S T 5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J 2 ybzbAb!bBb$i_k@bod[bpd]bqd^brd_bsd`btd;dCbDbEbFb'bK N ,qagX ^ _ (bO L A F B b x 9 y z C { D w P Q R E Y Z Gb)b*bddScU % ] 0 ` RctetmumIb]d^iehfhghhhihVcjhkhlhmhnhWcohphqhrhXcshthuhvhwhxhyhzhAhBhYcChDhxmym=qzm?qAmBmCmM DmHh@q[q]q^q_q`q{q|q}q~qEmTYFmUYGmRYHmVYWYSYImJmKmLmMmNmOmPmQmRmSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!m#m$m%m'm(m)m*m+m,m-m.m/m:m;m=m?m@m[m]m^m_m`m{m|mNx}mOx~manbncndnenfngnhnecqnHetnfcynJeVbDd' QeWbjbkbYb, - . / lb5cgcInReZb6jLdmb6c0b(jPdnbhc$ejiicOgPgUdVdQg/j'e(e)e*e7c+e:j,e-ejc8c9c!cWdkclcobmcncocpc4n.e3 : rc8n]esc^epbsi*ctc.n{e3b0d( df4bqbrb6b; = ? @ sb.cuc`nefvccogftb/c7bwk#dubwcBfMixc,g-g)d*d.gDkDfEfFfGf:cHfEkIfJfyc;c=c?c+dzcAcvbBcCcDcEcvoKf4 [ GczoQfHcSfwbZi{cIcMoVfJcToXfKc0oZfLc7o1fMc'o3fNc.o5fOc[o7fPcar9f|i!u
293cdef CUresult cuLibraryGetKernelCount(unsigned int* count, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
294 return _driver._cuLibraryGetKernelCount(count, lib)
297cdef CUresult cuLibraryEnumerateKernels(CUkernel* kernels, unsigned int numKernels, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil:
298 return _driver._cuLibraryEnumerateKernels(kernels, numKernels, lib)
301cdef CUresult cuLibraryGetModule(CUmodule* pMod, CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil:
302 return _driver._cuLibraryGetModule(pMod, library)
305cdef CUresult cuKernelGetFunction(CUfunction* pFunc, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
306 return _driver._cuKernelGetFunction(pFunc, kernel)
309cdef CUresult cuKernelGetLibrary(CUlibrary* pLib, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil:
310 return _driver._cuKernelGetLibrary(pLib, kernel)
313cdef CUresult cuLibraryGetGlobal(CUdeviceptr* dptr, size_t* bytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
314 return _driver._cuLibraryGetGlobal(dptr, bytes, library, name)
317cdef CUresult cuLibraryGetManaged(CUdeviceptr* dptr, size_t* bytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil:
318 return _driver._cuLibraryGetManaged(dptr, bytes, library, name)
321cdef CUresult cuLibraryGetUnifiedFunction(void** fptr, CUlibrary library, const char* symbol) except ?CUDA_ERROR_NOT_FOUND nogil:
322 return _driver._cuLibraryGetUnifiedFunction(fptr, library, symbol)
325cdef CUresult cuKernelGetAttribute(int* pi, CUfunction_attribute attrib, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
326 return _driver._cuKernelGetAttribute(pi, attrib, kernel, dev) 2,qagX xY=q?qyYzYSuTuUuVuWuXuYuZu0u1u2u3u4u5u6u7u8u9uAYBYCYDYEYFYGYHYIYJYKYLYMYNYOYPY
329cdef CUresult cuKernelSetAttribute(CUfunction_attribute attrib, int val, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
330 return _driver._cuKernelSetAttribute(attrib, val, kernel, dev)
333cdef CUresult cuKernelSetCacheConfig(CUkernel kernel, CUfunc_cache config, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
334 return _driver._cuKernelSetCacheConfig(kernel, config, dev)
337cdef CUresult cuKernelGetName(const char** name, CUkernel hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
338 return _driver._cuKernelGetName(name, hfunc) 2H2
341cdef CUresult cuKernelGetParamInfo(CUkernel kernel, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil:
342 return _driver._cuKernelGetParamInfo(kernel, paramIndex, paramOffset, paramSize) 2M Hh@q[q]q^q_q`q{q|q}q~qI2
345cdef CUresult cuMemGetInfo(size_t* free, size_t* total) except ?CUDA_ERROR_NOT_FOUND nogil:
346 return _driver._cuMemGetInfo_v2(free, total)
349cdef CUresult cuMemAlloc(CUdeviceptr* dptr, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil:
350 return _driver._cuMemAlloc_v2(dptr, bytesize) 2/i*xXY| YYZY0Y1Y2Y3Y4Y5Y6Y7Y8Y@d[dbl_d{bHxIxGrHrvpIrwpJrKrxpypLrMrNrzpOrApBpCpDpEpFpGpHpIpPrJpKpLpMpQrNpOpRrSrclvmcclpqlrl
353cdef CUresult cuMemAllocPitch(CUdeviceptr* dptr, size_t* pPitch, size_t WidthInBytes, size_t Height, unsigned int ElementSizeBytes) except ?CUDA_ERROR_NOT_FOUND nogil:
354 return _driver._cuMemAllocPitch_v2(dptr, pPitch, WidthInBytes, Height, ElementSizeBytes)
357cdef CUresult cuMemFree(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
358 return _driver._cuMemFree_v2(dptr) 2~ x 9 y z C { D w P Q R KELEMENE-qOEQESE,rUEVE/ireQbabbb+ RbSbsecbdbebfbgbhbhp*x-rXY| YYZY0Y1Y2Y3Y4Y5Y6Y7YIb:iue8Y@d[dbl_d{bHxkrIxJxKxGrHrvpIrwpJrKrxpypLrMrNrzpOrApBpCpDpEpFpGpHpIpPrJpKpLpMpQrNpOpRrSr6r7r9p8r!p9r!r#p$p#r$r%r%p'r'p(p)p*p+p,p-p.p/p(r:p;p=p?p)r@p[p*r+rcl{kvmcclpqlrl
361cdef CUresult cuMemGetAddressRange(CUdeviceptr* pbase, size_t* psize, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
362 return _driver._cuMemGetAddressRange_v2(pbase, psize, dptr)
365cdef CUresult cuMemAllocHost(void** pp, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil:
366 return _driver._cuMemAllocHost_v2(pp, bytesize) 2S 1 c d e f g h i j k l m n o p q r s t u v G H I J O L A F B b =bE Y Z % ] 0 ` HbV W IbehfhghhhihVcjhkhlhmhnhWcohphqhrhXcshthuhvhwhxhyhzhAhBhYcChDhbl_d{bjrLxMxTrUrPpVrQpWrXrRpSpYrZr0rTp1rUpVpWpXpYpZp0p1p2p2r3p4p5p6p3r7p8p4r5rclM
369cdef CUresult cuMemFreeHost(void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
370 return _driver._cuMemFreeHost(p) 2S 1 c d e f g h i j k l m n o p q r s t u v G H I J O L A F B b =bE Y Z 9Y!Y0 ` HbV W IbehfhghhhihVcjhkhlhmhnhWcohphqhrhXcshthuhvhwhxhyhzhAhBhYcChDhbl_d{bjrLxMxTrUrPpVrQpWrXrRpSpYrZr0rTp1rUpVpWpXpYpZp0p1p2p2r3p4p5p6p3r7p8p4r5rclccM
373cdef CUresult cuMemHostAlloc(void** pp, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
374 return _driver._cuMemHostAlloc(pp, bytesize, Flags) 29Y!Y
377cdef CUresult cuMemHostGetDevicePointer(CUdeviceptr* pdptr, void* p, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
378 return _driver._cuMemHostGetDevicePointer_v2(pdptr, p, Flags)
381cdef CUresult cuMemHostGetFlags(unsigned int* pFlags, void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
382 return _driver._cuMemHostGetFlags(pFlags, p)
385cdef CUresult cuMemAllocManaged(CUdeviceptr* dptr, size_t bytesize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
386 return _driver._cuMemAllocManaged(dptr, bytesize, flags) 2x 9 y z C { D w P Q R {p|p~paq-qompmqm,rcqdq% ] igQbabbb+ ~fRbSbcbdbebfbgbhbhp-rIb:iuebl_d{bkrJxKx6r7r9p8r!p9r!r#p$p#r$r%r%p'r'p(p)p*p+p,p-p.p/p(r:p;p=p?p)r@p[p*r+rcl{k
389cdef CUresult cuDeviceRegisterAsyncNotification(CUdevice device, CUasyncCallback callbackFunc, void* userData, CUasyncCallbackHandle* callback) except ?CUDA_ERROR_NOT_FOUND nogil:
390 return _driver._cuDeviceRegisterAsyncNotification(device, callbackFunc, userData, callback)
393cdef CUresult cuDeviceUnregisterAsyncNotification(CUdevice device, CUasyncCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
394 return _driver._cuDeviceUnregisterAsyncNotification(device, callback)
397cdef CUresult cuDeviceGetByPCIBusId(CUdevice* dev, const char* pciBusId) except ?CUDA_ERROR_NOT_FOUND nogil:
398 return _driver._cuDeviceGetByPCIBusId(dev, pciBusId)
401cdef CUresult cuDeviceGetPCIBusId(char* pciBusId, int len, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
402 return _driver._cuDeviceGetPCIBusId(pciBusId, len, dev)
405cdef CUresult cuIpcGetEventHandle(CUipcEventHandle* pHandle, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
406 return _driver._cuIpcGetEventHandle(pHandle, event) 2% ] bp]g!i#icpdpepfpxl;i.d/d
409cdef CUresult cuIpcOpenEventHandle(CUevent* phEvent, CUipcEventHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
410 return _driver._cuIpcOpenEventHandle(phEvent, handle)
413cdef CUresult cuIpcGetMemHandle(CUipcMemHandle* pHandle, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
414 return _driver._cuIpcGetMemHandle(pHandle, dptr)
417cdef CUresult cuIpcOpenMemHandle(CUdeviceptr* pdptr, CUipcMemHandle handle, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
418 return _driver._cuIpcOpenMemHandle_v2(pdptr, handle, Flags)
421cdef CUresult cuIpcCloseMemHandle(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
422 return _driver._cuIpcCloseMemHandle(dptr)
425cdef CUresult cuMemHostRegister(void* p, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
426 return _driver._cuMemHostRegister_v2(p, bytesize, Flags) 2oqpq
429cdef CUresult cuMemHostUnregister(void* p) except ?CUDA_ERROR_NOT_FOUND nogil:
430 return _driver._cuMemHostUnregister(p) 2oqpq
433cdef CUresult cuMemcpy(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
434 return _driver._cuMemcpy(dst, src, ByteCount)
437cdef CUresult cuMemcpyPeer(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
438 return _driver._cuMemcpyPeer(dstDevice, dstContext, srcDevice, srcContext, ByteCount)
441cdef CUresult cuMemcpyHtoD(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
442 return _driver._cuMemcpyHtoD_v2(dstDevice, srcHost, ByteCount) 2*x|
445cdef CUresult cuMemcpyDtoH(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
446 return _driver._cuMemcpyDtoH_v2(dstHost, srcDevice, ByteCount) 26 7 8 * K N *x|
449cdef CUresult cuMemcpyDtoD(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
450 return _driver._cuMemcpyDtoD_v2(dstDevice, srcDevice, ByteCount)
453cdef CUresult cuMemcpyDtoA(CUarray dstArray, size_t dstOffset, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
454 return _driver._cuMemcpyDtoA_v2(dstArray, dstOffset, srcDevice, ByteCount)
457cdef CUresult cuMemcpyAtoD(CUdeviceptr dstDevice, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
458 return _driver._cuMemcpyAtoD_v2(dstDevice, srcArray, srcOffset, ByteCount)
461cdef CUresult cuMemcpyHtoA(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
462 return _driver._cuMemcpyHtoA_v2(dstArray, dstOffset, srcHost, ByteCount)
465cdef CUresult cuMemcpyAtoH(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
466 return _driver._cuMemcpyAtoH_v2(dstHost, srcArray, srcOffset, ByteCount)
469cdef CUresult cuMemcpyAtoA(CUarray dstArray, size_t dstOffset, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil:
470 return _driver._cuMemcpyAtoA_v2(dstArray, dstOffset, srcArray, srcOffset, ByteCount)
473cdef CUresult cuMemcpy2D(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
474 return _driver._cuMemcpy2D_v2(pCopy)
477cdef CUresult cuMemcpy2DUnaligned(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
478 return _driver._cuMemcpy2DUnaligned_v2(pCopy)
481cdef CUresult cuMemcpy3D(const CUDA_MEMCPY3D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
482 return _driver._cuMemcpy3D_v2(pCopy)
485cdef CUresult cuMemcpy3DPeer(const CUDA_MEMCPY3D_PEER* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil:
486 return _driver._cuMemcpy3DPeer(pCopy)
489cdef CUresult cuMemcpyAsync(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
490 return _driver._cuMemcpyAsync(dst, src, ByteCount, hStream) 2x 9 y z C { D w P Q R % ] igQbabbb+ ~fRbSbcbdbebfbgbhbHbV W Ib:iue_d{bTbibUbM
493cdef CUresult cuMemcpyPeerAsync(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
494 return _driver._cuMemcpyPeerAsync(dstDevice, dstContext, srcDevice, srcContext, ByteCount, hStream)
497cdef CUresult cuMemcpyHtoDAsync(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
498 return _driver._cuMemcpyHtoDAsync_v2(dstDevice, srcHost, ByteCount, hStream)
501cdef CUresult cuMemcpyDtoHAsync(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
502 return _driver._cuMemcpyDtoHAsync_v2(dstHost, srcDevice, ByteCount, hStream) 2@d[dbg
505cdef CUresult cuMemcpyDtoDAsync(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
506 return _driver._cuMemcpyDtoDAsync_v2(dstDevice, srcDevice, ByteCount, hStream)
509cdef CUresult cuMemcpyHtoAAsync(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
510 return _driver._cuMemcpyHtoAAsync_v2(dstArray, dstOffset, srcHost, ByteCount, hStream)
513cdef CUresult cuMemcpyAtoHAsync(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
514 return _driver._cuMemcpyAtoHAsync_v2(dstHost, srcArray, srcOffset, ByteCount, hStream)
517cdef CUresult cuMemcpy2DAsync(const CUDA_MEMCPY2D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
518 return _driver._cuMemcpy2DAsync_v2(pCopy, hStream)
521cdef CUresult cuMemcpy3DAsync(const CUDA_MEMCPY3D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
522 return _driver._cuMemcpy3DAsync_v2(pCopy, hStream)
525cdef CUresult cuMemcpy3DPeerAsync(const CUDA_MEMCPY3D_PEER* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
526 return _driver._cuMemcpy3DPeerAsync(pCopy, hStream)
529cdef CUresult cuMemsetD8(CUdeviceptr dstDevice, unsigned char uc, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
530 return _driver._cuMemsetD8_v2(dstDevice, uc, N)
533cdef CUresult cuMemsetD16(CUdeviceptr dstDevice, unsigned short us, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
534 return _driver._cuMemsetD16_v2(dstDevice, us, N)
537cdef CUresult cuMemsetD32(CUdeviceptr dstDevice, unsigned int ui, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil:
538 return _driver._cuMemsetD32_v2(dstDevice, ui, N)
541cdef CUresult cuMemsetD2D8(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
542 return _driver._cuMemsetD2D8_v2(dstDevice, dstPitch, uc, Width, Height)
545cdef CUresult cuMemsetD2D16(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
546 return _driver._cuMemsetD2D16_v2(dstDevice, dstPitch, us, Width, Height)
549cdef CUresult cuMemsetD2D32(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil:
550 return _driver._cuMemsetD2D32_v2(dstDevice, dstPitch, ui, Width, Height)
553cdef CUresult cuMemsetD8Async(CUdeviceptr dstDevice, unsigned char uc, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
554 return _driver._cuMemsetD8Async(dstDevice, uc, N, hStream) 2K N x 9 y z vpypApBpCpJpKpPpSpUpVpWp3p4p9p$p'p(p)p:p;p
557cdef CUresult cuMemsetD16Async(CUdeviceptr dstDevice, unsigned short us, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
558 return _driver._cuMemsetD16Async(dstDevice, us, N, hStream) 2wpDpEpFpLpMpQpXpYpZp5p6p!p*p+p,p=p?p
561cdef CUresult cuMemsetD32Async(CUdeviceptr dstDevice, unsigned int ui, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
562 return _driver._cuMemsetD32Async(dstDevice, ui, N, hStream) 2xpzpGpHpIpNpOpRpTp0p1p2p7p8p#p%p-p.p/p@p[p
565cdef CUresult cuMemsetD2D8Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
566 return _driver._cuMemsetD2D8Async(dstDevice, dstPitch, uc, Width, Height, hStream)
569cdef CUresult cuMemsetD2D16Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
570 return _driver._cuMemsetD2D16Async(dstDevice, dstPitch, us, Width, Height, hStream)
573cdef CUresult cuMemsetD2D32Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
574 return _driver._cuMemsetD2D32Async(dstDevice, dstPitch, ui, Width, Height, hStream)
577cdef CUresult cuArrayCreate(CUarray* pHandle, const CUDA_ARRAY_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
578 return _driver._cuArrayCreate_v2(pHandle, pAllocateArray) 2#Y
581cdef CUresult cuArrayGetDescriptor(CUDA_ARRAY_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
582 return _driver._cuArrayGetDescriptor_v2(pArrayDescriptor, hArray)
585cdef CUresult cuArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUarray array) except ?CUDA_ERROR_NOT_FOUND nogil:
586 return _driver._cuArrayGetSparseProperties(sparseProperties, array)
589cdef CUresult cuMipmappedArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUmipmappedArray mipmap) except ?CUDA_ERROR_NOT_FOUND nogil:
590 return _driver._cuMipmappedArrayGetSparseProperties(sparseProperties, mipmap)
593cdef CUresult cuArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUarray array, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
594 return _driver._cuArrayGetMemoryRequirements(memoryRequirements, array, device)
597cdef CUresult cuMipmappedArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUmipmappedArray mipmap, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
598 return _driver._cuMipmappedArrayGetMemoryRequirements(memoryRequirements, mipmap, device)
601cdef CUresult cuArrayGetPlane(CUarray* pPlaneArray, CUarray hArray, unsigned int planeIdx) except ?CUDA_ERROR_NOT_FOUND nogil:
602 return _driver._cuArrayGetPlane(pPlaneArray, hArray, planeIdx)
605cdef CUresult cuArrayDestroy(CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
606 return _driver._cuArrayDestroy(hArray) 2#Y
609cdef CUresult cuArray3DCreate(CUarray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil:
610 return _driver._cuArray3DCreate_v2(pHandle, pAllocateArray)
613cdef CUresult cuArray3DGetDescriptor(CUDA_ARRAY3D_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil:
614 return _driver._cuArray3DGetDescriptor_v2(pArrayDescriptor, hArray)
617cdef CUresult cuMipmappedArrayCreate(CUmipmappedArray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc, unsigned int numMipmapLevels) except ?CUDA_ERROR_NOT_FOUND nogil:
618 return _driver._cuMipmappedArrayCreate(pHandle, pMipmappedArrayDesc, numMipmapLevels)
621cdef CUresult cuMipmappedArrayGetLevel(CUarray* pLevelArray, CUmipmappedArray hMipmappedArray, unsigned int level) except ?CUDA_ERROR_NOT_FOUND nogil:
622 return _driver._cuMipmappedArrayGetLevel(pLevelArray, hMipmappedArray, level)
625cdef CUresult cuMipmappedArrayDestroy(CUmipmappedArray hMipmappedArray) except ?CUDA_ERROR_NOT_FOUND nogil:
626 return _driver._cuMipmappedArrayDestroy(hMipmappedArray)
629cdef CUresult cuMemGetHandleForAddressRange(void* handle, CUdeviceptr dptr, size_t size, CUmemRangeHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
630 return _driver._cuMemGetHandleForAddressRange(handle, dptr, size, handleType, flags)
633cdef CUresult cuMemBatchDecompressAsync(CUmemDecompressParams* paramsArray, size_t count, unsigned int flags, size_t* errorIndex, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
634 return _driver._cuMemBatchDecompressAsync(paramsArray, count, flags, errorIndex, stream)
637cdef CUresult cuMemAddressReserve(CUdeviceptr* ptr, size_t size, size_t alignment, CUdeviceptr addr, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
638 return _driver._cuMemAddressReserve(ptr, size, alignment, addr, flags) 2edfd} gd
641cdef CUresult cuMemAddressFree(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
642 return _driver._cuMemAddressFree(ptr, size) 2edfd} gd
645cdef CUresult cuMemCreate(CUmemGenericAllocationHandle* handle, size_t size, const CUmemAllocationProp* prop, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
646 return _driver._cuMemCreate(handle, size, prop, flags) 2edfd} gd
649cdef CUresult cuMemRelease(CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
650 return _driver._cuMemRelease(handle) 2edfd} gd
653cdef CUresult cuMemMap(CUdeviceptr ptr, size_t size, size_t offset, CUmemGenericAllocationHandle handle, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
654 return _driver._cuMemMap(ptr, size, offset, handle, flags) 2edfd} gd
657cdef CUresult cuMemMapArrayAsync(CUarrayMapInfo* mapInfoList, unsigned int count, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
658 return _driver._cuMemMapArrayAsync(mapInfoList, count, hStream)
661cdef CUresult cuMemUnmap(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
662 return _driver._cuMemUnmap(ptr, size) 2edfd} gd
665cdef CUresult cuMemSetAccess(CUdeviceptr ptr, size_t size, const CUmemAccessDesc* desc, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
666 return _driver._cuMemSetAccess(ptr, size, desc, count) 2edfd} gd
669cdef CUresult cuMemGetAccess(unsigned long long* flags, const CUmemLocation* location, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
670 return _driver._cuMemGetAccess(flags, location, ptr)
673cdef CUresult cuMemExportToShareableHandle(void* shareableHandle, CUmemGenericAllocationHandle handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
674 return _driver._cuMemExportToShareableHandle(shareableHandle, handle, handleType, flags)
677cdef CUresult cuMemImportFromShareableHandle(CUmemGenericAllocationHandle* handle, void* osHandle, CUmemAllocationHandleType shHandleType) except ?CUDA_ERROR_NOT_FOUND nogil:
678 return _driver._cuMemImportFromShareableHandle(handle, osHandle, shHandleType)
681cdef CUresult cuMemGetAllocationGranularity(size_t* granularity, const CUmemAllocationProp* prop, CUmemAllocationGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil:
682 return _driver._cuMemGetAllocationGranularity(granularity, prop, option) 2edfd} gd
685cdef CUresult cuMemGetAllocationPropertiesFromHandle(CUmemAllocationProp* prop, CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil:
686 return _driver._cuMemGetAllocationPropertiesFromHandle(prop, handle)
689cdef CUresult cuMemRetainAllocationHandle(CUmemGenericAllocationHandle* handle, void* addr) except ?CUDA_ERROR_NOT_FOUND nogil:
690 return _driver._cuMemRetainAllocationHandle(handle, addr) 2edfd} gd
693cdef CUresult cuMemFreeAsync(CUdeviceptr dptr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
694 return _driver._cuMemFreeAsync(dptr, hStream) 2~ K +b,b-bkdldmdx 9 y z C { D w P Q R NbObPb! # $ dg`d4LPEndRETEegfgqprpsptpupoepeqegghg+x,x-x.x/x:x;x=x?x@x[x]xreQbabbb+ RbSbse6hcbdbebfbgbhb^g_gHbV W kglg+i,iTb|b|kib-iud}kvd}bwd~bZcxdydaczdbcAd0cBdJjccCd.i~kUbdcGeM 6E:E?E^u_u`u{ubrcr|u}u~uavbvqFcvrFdvevsFfvgvhvMF2Ftv'vyH|v}v~vawfrgrbwcwdwewfwZHgw0Hhwiw1Hjwkwlw.HaIxw+w}c?b7J=JgKyKQK8K?KhL#f$forpr%f'f(f)f*fqr+f,f-frr.fsr/ftr:f;fur=fvr?fwr@fxr[fyrzr]f^f_f`f{fAr|fBr}fip
697cdef CUresult cuMemAllocAsync(CUdeviceptr* dptr, size_t bytesize, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
698 return _driver._cuMemAllocAsync(dptr, bytesize, hStream) 2kdldmdx y z C D w P Q R NbObPb! # $
701cdef CUresult cuMemPoolTrimTo(CUmemoryPool pool, size_t minBytesToKeep) except ?CUDA_ERROR_NOT_FOUND nogil:
702 return _driver._cuMemPoolTrimTo(pool, minBytesToKeep)
705cdef CUresult cuMemPoolSetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
706 return _driver._cuMemPoolSetAttribute(pool, attr, value) 2^x3c
709cdef CUresult cuMemPoolGetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
710 return _driver._cuMemPoolGetAttribute(pool, attr, value) 2K N +b,b-bx 9 y z C { D w ^x^g_gHbV W kglg+i,i$zFC-i!hvevd}b#hwe$hxe%hye'hzewd~b(hmgngZcogpgqgrgxdsg)hAeydac*hBe+hCe,hDe-hEezdbc.hFetgug/hAd0cBdCdM KjPjQjOe' PeEd1c2c3c[hFdGdHdQeWbWjXb4cAg]hIdJdXj{hciXg}jbf( cf1d^d,c2dxi3d4d5ddf4bek5b-cyizi6d7dfkkkFi;gRkWk1k6k#k)k.k?k#f$f%f'f(f)f*f+f,f-f.f/f:f;f=f?f@f[f]f^f_f`f{f|f}fip
713cdef CUresult cuMemPoolSetAccess(CUmemoryPool pool, const CUmemAccessDesc* map, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
714 return _driver._cuMemPoolSetAccess(pool, map, count) 2~ lzmznzoeozpzqzperzqeszgghgtzuzvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzreQbabbb+ RbSbse6hcbdbebfbgbhbTbwt|b7h8h9hibud!hvevd}b#hwe$hxe%hye'hzewd~b(hmgngZcogpgqgrgxdsg)hAeydac*hBe+hCe,hDe-hEezdbc.hFetgug/hAd0cBdJjccUbdcGewm:h;hM injnknln}c?b
717cdef CUresult cuMemPoolGetAccess(CUmemAccess_flags* flags, CUmemoryPool memPool, CUmemLocation* location) except ?CUDA_ERROR_NOT_FOUND nogil:
718 return _driver._cuMemPoolGetAccess(flags, memPool, location) 2FC
721cdef CUresult cuMemPoolCreate(CUmemoryPool* pool, const CUmemPoolProps* poolProps) except ?CUDA_ERROR_NOT_FOUND nogil:
722 return _driver._cuMemPoolCreate(pool, poolProps) 2yLnxapzLoeoxALpxpeBLqezjCL.q8q/qDLqxELFLGLHLILJLKLLLMLNLOLPLrxsxtxuxvxwxxxgpyxzxAxBxQLCxrm:qRLDxSLEx9q;q+ ~fTLFxULGxVLAjcbdbebfbgbhb^xTbwt|b7h8h9hibud!hvevd}b#hwe$hxe%hye'hzewd~b(hmgngZcogpgqgrgxdsg)hAeydac*hBe+hCe,hDe-hEezdbc.hFetgug/hAd0cBdJjUbdcGewm:h;hinjnknln}c?b
725cdef CUresult cuMemPoolDestroy(CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
726 return _driver._cuMemPoolDestroy(pool) 2~ lzmznzoeozpzqzperzqeszgghgtzuzvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzreQbabbb+ RbSbse6hcbdbebfbgbhb^xTbwt|b7h8h9hibud!hvevd}b#hwe$hxe%hye'hzewd~b(hmgngZcogpgqgrgxdsg)hAeydac*hBe+hCe,hDe-hEezdbc.hFetgug/hAd0cBdJjccUbdcGewm:h;hM injnknln}c?b
729cdef CUresult cuMemAllocFromPoolAsync(CUdeviceptr* dptr, size_t bytesize, CUmemoryPool pool, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
730 return _driver._cuMemAllocFromPoolAsync(dptr, bytesize, pool, hStream) 2K N +b,b-bx 9 y z C { D w dg`d4LwjndxjyjegfgqprpsptpupapoekqIupeqe% ] gghg+x,x-x.x/x:x;x=x?x@x[x]xlqreJuKumqLuigQbabbb+ ~fRbSbse6hnq7qcbdbebfbgbhb^g_gHbV W kglg+i,iTb|b|kib-iud}kvd}bwd~bZcxdydaczdbcAd0cBdJjCd.i~kUbdcGeM KjPjQjOe' PeEd1c2c3c[hFdGdHdQeWbWjXb4cAg]hIdJdXj{hciXg}jbf( cf1d^d,c2dxi3d4d5ddf4bek5b-cyizi6d7dfkkkFi;g}c?bRkWk1k6k#k)k.k?k#f$forpr%f'f(f)f*fqr+f,f-frr.fsr/ftr:f;fur=fvr?fwr@fxr[fyrzr]f^f_f`f{fAr|fBr}fip
733cdef CUresult cuMemPoolExportToShareableHandle(void* handle_out, CUmemoryPool pool, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
734 return _driver._cuMemPoolExportToShareableHandle(handle_out, pool, handleType, flags) 2yLnxapzLoeoxALpxpeBLqezjCL.q8q/qDLqxELFLGLHLILJLKLLLMLNLOLPLrxsxtxuxvxwxxxgpyxzxAxBxQLCxrm:qRLDxSLEx9q;q+ ~fTLFxULGxVLAjcbdbebfbgbhbve}bwexeyeze~bmgAeacBeCeDeEebcFedc:h;hinjnknln}c?b
737cdef CUresult cuMemPoolImportFromShareableHandle(CUmemoryPool* pool_out, void* handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
738 return _driver._cuMemPoolImportFromShareableHandle(pool_out, handle, handleType, flags)
741cdef CUresult cuMemPoolExportPointer(CUmemPoolPtrExportData* shareData_out, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
742 return _driver._cuMemPoolExportPointer(shareData_out, ptr) 2apoekqIupeqe% ] gghg+x,x-x.x/x:x;x=x?x@x[x]xlqreJuKumqLuigQbabbb+ ~fRbSbse6hnq7qcbdbebfbgbhbdc}c?b
745cdef CUresult cuMemPoolImportPointer(CUdeviceptr* ptr_out, CUmemoryPool pool, CUmemPoolPtrExportData* shareData) except ?CUDA_ERROR_NOT_FOUND nogil:
746 return _driver._cuMemPoolImportPointer(ptr_out, pool, shareData)
749cdef CUresult cuMulticastCreate(CUmemGenericAllocationHandle* mcHandle, const CUmulticastObjectProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
750 return _driver._cuMulticastCreate(mcHandle, prop)
753cdef CUresult cuMulticastAddDevice(CUmemGenericAllocationHandle mcHandle, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
754 return _driver._cuMulticastAddDevice(mcHandle, dev)
757cdef CUresult cuMulticastBindMem(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUmemGenericAllocationHandle memHandle, size_t memOffset, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
758 return _driver._cuMulticastBindMem(mcHandle, mcOffset, memHandle, memOffset, size, flags)
761cdef CUresult cuMulticastBindAddr(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
762 return _driver._cuMulticastBindAddr(mcHandle, mcOffset, memptr, size, flags)
765cdef CUresult cuMulticastUnbind(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
766 return _driver._cuMulticastUnbind(mcHandle, dev, mcOffset, size)
769cdef CUresult cuMulticastGetGranularity(size_t* granularity, const CUmulticastObjectProp* prop, CUmulticastGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil:
770 return _driver._cuMulticastGetGranularity(granularity, prop, option)
773cdef CUresult cuPointerGetAttribute(void* data, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
774 return _driver._cuPointerGetAttribute(data, attribute, ptr) 26 7 8 * }dbeeehekene-rIeKeNeXbKdSeMdWeQdTd%e7cob/e3 1b2bqc#c$c%c'cYdZd_e+c|eaf5b8dffhflf$d(dCf:cvbLf4 8b9bFc@c[c]c^c-dRfTf|cWfYf0f2f4f6f8f!f
777cdef CUresult cuMemPrefetchAsync(CUdeviceptr devPtr, size_t count, CUmemLocation location, unsigned int flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
778 return _driver._cuMemPrefetchAsync_v2(devPtr, count, location, flags, hStream) 2tlulndvlwl
781cdef CUresult cuMemAdvise(CUdeviceptr devPtr, size_t count, CUmem_advise advice, CUmemLocation location) except ?CUDA_ERROR_NOT_FOUND nogil:
782 return _driver._cuMemAdvise_v2(devPtr, count, advice, location) 2ssnm}p$Y,r5L6Lhp
785cdef CUresult cuMemRangeGetAttribute(void* data, size_t dataSize, CUmem_range_attribute attribute, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
786 return _driver._cuMemRangeGetAttribute(data, dataSize, attribute, devPtr, count) 2`dssnm}pndvlwl,r5L6Legfghp
789cdef CUresult cuMemRangeGetAttributes(void** data, size_t* dataSizes, CUmem_range_attribute* attributes, size_t numAttributes, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
790 return _driver._cuMemRangeGetAttributes(data, dataSizes, attributes, numAttributes, devPtr, count) 2hp
793cdef CUresult cuPointerSetAttribute(const void* value, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
794 return _driver._cuPointerSetAttribute(value, attribute, ptr) 2-r
797cdef CUresult cuPointerGetAttributes(unsigned int numAttributes, CUpointer_attribute* attributes, void** data, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil:
798 return _driver._cuPointerGetAttributes(numAttributes, attributes, data, ptr) 2S 1 c d e f g h i j k l m n o p q r s t u v G H I J O L A F B b =bE Y Z dg`dssnm}p$YtlulndvlwlDrEr,r5L6Legfg/i-rJ2HbV W ehfhghhhihVcjhkhlhmhnhWcohphqhrhXcshthuhvhwhxhyhzhAhBhYcChDhjrkrkglgK2JxKxLxMxoqpq{k|bCd.iM L2M2N2O2P2Q2R2S2T2U2
801cdef CUresult cuStreamCreate(CUstream* phStream, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
802 return _driver._cuStreamCreate(phStream, Flags) 2`i7LGh| %Y@d[d%i'i(ibg)i*i
805cdef CUresult cuStreamCreateWithPriority(CUstream* phStream, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil:
806 return _driver._cuStreamCreateWithPriority(phStream, flags, priority) 2JbKbcgS T ?i5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J hd~cadbd:d2 .bidjdybzbAb!bBb6 7 8 * #b$b%bQccd/b:bLbMbK N X ^ _ ;bO L A F B b +b,b-bkdldmdx 9 y z C { D w P Q R NbObPb! # $ E Y Z Gb)b*bddScU dg`dtlulndvlwlDrEregfgqprpsptpup/i% ] bp]g!i#icpdpepfpxl1L2LigQbabbb+ ~fRbSbcbdbebfbgbhbRxSxTxUxVxWxXxTc0 Ucflglhliljlkl` llmlnlolpl]iEhRc`gjp{g|gkp}g~gahjgbhchdhalIb:iue]d^i_d{bGrHrvpIrwpJrKrxpypLrMrNrzpOrApBpCpDpEpFpGpHpIpPrJpKpLpMpQrNpOpRrSrTrUrPpVrQpWrXrRpSpYrZr0rTp1rUpVpWpXpYpZp0p1p2p2r3p4p5p6p3r7p8p4r5r6r7r9p8r!p9r!r#p$p#r$r%r%p'r'p(p)p*p+p,p-p.p/p(r:p;p=p?p)r@p[p*r+rTbiblpUbqlrlM ;iHtItJtyqpiXgpb{jPtYgCqZg0g1gDqdlqirisi*cQt+c`e|jEqtiuiRtUtVi;gwbQkYt=gPq?g@g[gQqWiXiYiZi{cZt|cUfGoRq0i1i.d/d4t5t6t7t8t9t$t(tYxZx0x1x2x3xCr4x5x6x7x8x9x!x#x$xsl%xnrFr'xFh(x
809cdef CUresult cuStreamGetPriority(CUstream hStream, int* priority) except ?CUDA_ERROR_NOT_FOUND nogil:
810 return _driver._cuStreamGetPriority(hStream, priority)
813cdef CUresult cuStreamGetDevice(CUstream hStream, CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil:
814 return _driver._cuStreamGetDevice(hStream, device)
817cdef CUresult cuStreamGetFlags(CUstream hStream, unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
818 return _driver._cuStreamGetFlags(hStream, flags)
821cdef CUresult cuStreamGetId(CUstream hStream, unsigned long long* streamId) except ?CUDA_ERROR_NOT_FOUND nogil:
822 return _driver._cuStreamGetId(hStream, streamId)
825cdef CUresult cuStreamGetCtx(CUstream hStream, CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil:
826 return _driver._cuStreamGetCtx(hStream, pctx)
829cdef CUresult cuStreamGetCtx_v2(CUstream hStream, CUcontext* pCtx, CUgreenCtx* pGreenCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
830 return _driver._cuStreamGetCtx_v2(hStream, pCtx, pGreenCtx)
833cdef CUresult cuStreamWaitEvent(CUstream hStream, CUevent hEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
834 return _driver._cuStreamWaitEvent(hStream, hEvent, Flags) 2T 5 c d e f g h i j k l m n o p q r s t u v U Fh
837cdef CUresult cuStreamAddCallback(CUstream hStream, CUstreamCallback callback, void* userData, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
838 return _driver._cuStreamAddCallback(hStream, callback, userData, flags)
841cdef CUresult cuStreamBeginCapture(CUstream hStream, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil:
842 return _driver._cuStreamBeginCapture_v2(hStream, mode) 2JbKbcgS T ?i5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J +b,b-bkdldmdx y z C D w P Q R NbObPb! # $ E Y Gb)b*bddScU
845cdef CUresult cuStreamBeginCaptureToGraph(CUstream hStream, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil:
846 return _driver._cuStreamBeginCaptureToGraph(hStream, hGraph, dependencies, dependencyData, numDependencies, mode) 1cdefghijklmnopqrstuvGHIJEU
849cdef CUresult cuThreadExchangeStreamCaptureMode(CUstreamCaptureMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil:
850 return _driver._cuThreadExchangeStreamCaptureMode(mode)
853cdef CUresult cuStreamEndCapture(CUstream hStream, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
854 return _driver._cuStreamEndCapture(hStream, phGraph) 2JbKbcgS T ?i5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J +b,b-bkdldmdx y z C D w P Q R NbObPb! # $ E Y Gb)b*bddScU
857cdef CUresult cuStreamIsCapturing(CUstream hStream, CUstreamCaptureStatus* captureStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
858 return _driver._cuStreamIsCapturing(hStream, captureStatus) 2K N +b,b-bkdldmdx 9 y z C { D w P Q R NbObPb! # $ dg`d4LwjndxjyjegfgqprpsptpupapoekqIupeqe% ] gghg+x,x-x.x/x:x;x=x?x@x[x]xlqreJuKumqLuigQbabbb+ ~fRbSbse6hnq7qcbdbebfbgbhb^g_gHbV W kglg+i,iTb|b|kib-iud}kvd}bwd~bZcxdydaczdbcAd0cBdJjCd.i~kUbdcGeM KjPjQjOe' PeEd1c2c3c[hFdGdHdQeWbWjXb4cAg]hIdJdXj{hciXg}jbf( cf1d^d,c2dxi3d4d5ddf4bek5b-cyizi6d7dfkkkFi;g}c?bRkWk1k6k#k)k.k?k#f$forpr%f'f(f)f*fqr+f,f-frr.fsr/ftr:f;fur=fvr?fwr@fxr[fyrzr]f^f_f`f{fAr|fBr}fip
861cdef CUresult cuStreamGetCaptureInfo(CUstream hStream, CUstreamCaptureStatus* captureStatus_out, cuuint64_t* id_out, CUgraph* graph_out, const CUgraphNode** dependencies_out, const CUgraphEdgeData** edgeData_out, size_t* numDependencies_out) except ?CUDA_ERROR_NOT_FOUND nogil:
862 return _driver._cuStreamGetCaptureInfo_v3(hStream, captureStatus_out, id_out, graph_out, dependencies_out, edgeData_out, numDependencies_out) 2JbKbcgS T ?i5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J +b,b-bkdldmdx y z C D w P Q R NbObPb! # $ E Y Gb)b*bddScU
865cdef CUresult cuStreamUpdateCaptureDependencies(CUstream hStream, CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
866 return _driver._cuStreamUpdateCaptureDependencies_v2(hStream, dependencies, dependencyData, numDependencies, flags) 1ScdefghijklmnopqrstuvGHIJEU
869cdef CUresult cuStreamAttachMemAsync(CUstream hStream, CUdeviceptr dptr, size_t length, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
870 return _driver._cuStreamAttachMemAsync(hStream, dptr, length, flags)
873cdef CUresult cuStreamQuery(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
874 return _driver._cuStreamQuery(hStream)
877cdef CUresult cuStreamSynchronize(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
878 return _driver._cuStreamSynchronize(hStream) 2JbKbS T 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J hd~cadbd:d2 .bidjdybzbAb!bBb6 7 8 * #b$b%bQccd/b:bLbMbK N X ^ _ ;bO L A F B b =bx 9 y z C { D w P Q R NbObPb! # $ E Y Z dg`dtlulndvlwlegfg| Tc0 Uc` HbV W _iIb@d[d%i'i(ibg)i*i]d^iehfhghhhihVcjhkhlhmhnhWcohphqhrhXcshthuhvhwhxhyhzhAhBhYcChDhV2ccqlrlM FrFh
881cdef CUresult cuStreamDestroy(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
882 return _driver._cuStreamDestroy_v2(hStream) 2JbKbcgS T ?i5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J hd~cadbd:d2 .bidjdybzbAb!bBb6 7 8 * #b$b%bQccd/b:b~ LbMbK N X ^ _ ;bO L A F B b +b,b-bkdldmdx 9 y z C { D w P Q R NbObPb! # $ E Y Z Gb)b*bddScU dg`dtlulndvlwlDrEregfgqprpsptpup/i]g!i#ixl1L2LreQbabbb+ RbSbsecbdbebfbgbhbRxSxTxUxVxWx`i7LGh| XxTc0 Ucflglhliljlkl` llmlnlolpl]iEhRc`g{g|gkp}g~gahbhchdh)xHbV W 3L_iIb:iue%Y@d[d%i'i(ibg)i*i]d^i_d{bGrHrvpIrwpJrKrxpypLrMrNrzpOrApBpCpDpEpFpGpHpIpPrJpKpLpMpQrNpOpRrSrTrUrPpVrQpWrXrRpSpYrZr0rTp1rUpVpWpXpYpZp0p1p2p2r3p4p5p6p3r7p8p4r5r6r7r9p8r!p9r!r#p$p#r$r%r%p'r'p(p)p*p+p,p-p.p/p(r:p;p=p?p)r@p[p*r+rTbibccUbqlrlM ;i-E;EdF)F%v'v(v)vsH*v+vdrer,v-v.v/v:vtH;vuH=v?vvH@v[v]vMHoI*w+w,w-w1J.w/whrir:w;w=w?w@w2J[w3J]w^w4J_w`w{w.d/d.JcKuKMK4K/KdLvLYxZx0x1x2x3xCr4x5x6x7x8x9x!x#x$xsl%xnrFr'xFh(x
885cdef CUresult cuStreamCopyAttributes(CUstream dst, CUstream src) except ?CUDA_ERROR_NOT_FOUND nogil:
886 return _driver._cuStreamCopyAttributes(dst, src)
889cdef CUresult cuStreamGetAttribute(CUstream hStream, CUstreamAttrID attr, CUstreamAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
890 return _driver._cuStreamGetAttribute(hStream, attr, value_out)
893cdef CUresult cuStreamSetAttribute(CUstream hStream, CUstreamAttrID attr, const CUstreamAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
894 return _driver._cuStreamSetAttribute(hStream, attr, value)
897cdef CUresult cuEventCreate(CUevent* phEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
898 return _driver._cuEventCreate(phEvent, Flags) 2T 5 c d e f g h i j k l m n o p q r s t u v .b{d|d~daecedefegeiejeleme~ =d@iLbMb?d[iX U % ] bp]g!i#icpdpepfpxlYLTc0 UcZLsm0Lflglhliljlkl` llmlnlolpl]iEhRc_i'Y;i)zMjNj-zSjTjLeMe1c2cjbkbCgDgZj0jKt}h~hNdOdmrci0bNn@zdi!j#jeiNt$j%j'j(jPd[zQdIgOnOt)j*jfigiZe0e1e2ehi3e4e5e6eRdSd,j-jUdVd8c9c=j?j1b2b(c)c@e[e^j_jCqZg0g`zakbk}e~e^d,cqbrb8g9ghkikaAmknk9d!dqkFi7bfodAGirkskHiVttkukvkwk#deA$d%gKqWtxkykIiJiofpfqfrfKisftfufvf%d'dAkBk)d*d;c=cGkHk8b9b_c`c/g:gNkOkPq?g@g.d/djATkUkmAYkZkqA3k4kuA8k9kyA%k'kCA+k,kFA:k;kIA[k]kslFh
901cdef CUresult cuEventRecord(CUevent hEvent, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
902 return _driver._cuEventRecord(hEvent, hStream) 2T 5 c d e f g h i j k l m n o p q r s t u v U % ] bp]g!i#icpdpepfpxlTc0 Ucflglhliljlkl` llmlnlolpl]iEhRc_i;i.d/dslFh
905cdef CUresult cuEventRecordWithFlags(CUevent hEvent, CUstream hStream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
906 return _driver._cuEventRecordWithFlags(hEvent, hStream, flags)
909cdef CUresult cuEventQuery(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
910 return _driver._cuEventQuery(hEvent) 2~ =d?d` ]iEh
913cdef CUresult cuEventSynchronize(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
914 return _driver._cuEventSynchronize(hEvent) 20 ` EhRc_i
917cdef CUresult cuEventDestroy(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
918 return _driver._cuEventDestroy_v2(hEvent) 2T 5 c d e f g h i j k l m n o p q r s t u v #u$u%u'u(u)u*u+u,u-u.u/u:u~ =d@i?d[iU !i#ixlYLTc0 UcZLsm0Lflglhliljlkl` llmlnlolpl]iEhRc_i'Ycc;i!E;u=u^E?u@u[u]ubrcrivjvkvlvmvnv6Fovpvqvrvsvtvuvvv^FwvxvyvzvAvBvCvDv_FEv`FFvGv{FHvIvJvKvLvMvNvOvPvQvRvSvTvUvVvWvXvYvZv0v1v2v3v4v5v6v7v8v9v!v#v$v+vdrerCH^v_v`v{vfrgrmwnwowpwqwrweIswtwuwvwwwxwywzwCIAwBwCwDwEwFwGwHwDIIwEIJwKwFILwMwNwOwPwQwRwSwTwUwVwWwXwYwZw0w1w2w3w4w5w6w7w8w9w!w#w$w%w'w(w)w/whrir.d/d#J|w}w]J~waxkKbxcxCKdxexUKfxgx$Khxix^KjxkxlLlxmxslFh
921cdef CUresult cuEventElapsedTime(float* pMilliseconds, CUevent hStart, CUevent hEnd) except ?CUDA_ERROR_NOT_FOUND nogil:
922 return _driver._cuEventElapsedTime_v2(pMilliseconds, hStart, hEnd) 2Tc0 UcRc
925cdef CUresult cuImportExternalMemory(CUexternalMemory* extMem_out, const CUDA_EXTERNAL_MEMORY_HANDLE_DESC* memHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
926 return _driver._cuImportExternalMemory(extMem_out, memHandleDesc)
929cdef CUresult cuExternalMemoryGetMappedBuffer(CUdeviceptr* devPtr, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_BUFFER_DESC* bufferDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
930 return _driver._cuExternalMemoryGetMappedBuffer(devPtr, extMem, bufferDesc)
933cdef CUresult cuExternalMemoryGetMappedMipmappedArray(CUmipmappedArray* mipmap, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC* mipmapDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
934 return _driver._cuExternalMemoryGetMappedMipmappedArray(mipmap, extMem, mipmapDesc)
937cdef CUresult cuDestroyExternalMemory(CUexternalMemory extMem) except ?CUDA_ERROR_NOT_FOUND nogil:
938 return _driver._cuDestroyExternalMemory(extMem)
941cdef CUresult cuImportExternalSemaphore(CUexternalSemaphore* extSem_out, const CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC* semHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
942 return _driver._cuImportExternalSemaphore(extSem_out, semHandleDesc)
945cdef CUresult cuSignalExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
946 return _driver._cuSignalExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream)
949cdef CUresult cuWaitExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil:
950 return _driver._cuWaitExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream)
953cdef CUresult cuDestroyExternalSemaphore(CUexternalSemaphore extSem) except ?CUDA_ERROR_NOT_FOUND nogil:
954 return _driver._cuDestroyExternalSemaphore(extSem)
957cdef CUresult cuStreamWaitValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
958 return _driver._cuStreamWaitValue32_v2(stream, addr, value, flags)
961cdef CUresult cuStreamWaitValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
962 return _driver._cuStreamWaitValue64_v2(stream, addr, value, flags)
965cdef CUresult cuStreamWriteValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
966 return _driver._cuStreamWriteValue32_v2(stream, addr, value, flags)
969cdef CUresult cuStreamWriteValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
970 return _driver._cuStreamWriteValue64_v2(stream, addr, value, flags)
973cdef CUresult cuStreamBatchMemOp(CUstream stream, unsigned int count, CUstreamBatchMemOpParams* paramArray, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
974 return _driver._cuStreamBatchMemOp_v2(stream, count, paramArray, flags)
977cdef CUresult cuFuncGetAttribute(int* pi, CUfunction_attribute attrib, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
978 return _driver._cuFuncGetAttribute(pi, attrib, hfunc)
981cdef CUresult cuFuncSetAttribute(CUfunction hfunc, CUfunction_attribute attrib, int value) except ?CUDA_ERROR_NOT_FOUND nogil:
982 return _driver._cuFuncSetAttribute(hfunc, attrib, value)
985cdef CUresult cuFuncSetCacheConfig(CUfunction hfunc, CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil:
986 return _driver._cuFuncSetCacheConfig(hfunc, config)
989cdef CUresult cuFuncGetModule(CUmodule* hmod, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
990 return _driver._cuFuncGetModule(hmod, hfunc)
993cdef CUresult cuFuncGetName(const char** name, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil:
994 return _driver._cuFuncGetName(name, hfunc) 2W2
997cdef CUresult cuFuncGetParamInfo(CUfunction func, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil:
998 return _driver._cuFuncGetParamInfo(func, paramIndex, paramOffset, paramSize)
1001cdef CUresult cuFuncIsLoaded(CUfunctionLoadingState* state, CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
1002 return _driver._cuFuncIsLoaded(state, function)
1005cdef CUresult cuFuncLoad(CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil:
1006 return _driver._cuFuncLoad(function)
1009cdef CUresult cuLaunchKernel(CUfunction f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, CUstream hStream, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil:
1010 return _driver._cuLaunchKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams, extra) 2@d[d%i'i(ibg)i*i
1013cdef CUresult cuLaunchKernelEx(const CUlaunchConfig* config, CUfunction f, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil:
1014 return _driver._cuLaunchKernelEx(config, f, kernelParams, extra) 2S T 5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J x 9 y z C { D w P Q R E Y Gb)b*bddScU % ] 0 ` RcHbV W Ib]d^iehfhghhhihVcjhkhlhmhnhWcohphqhrhXcshthuhvhwhxhyhzhAhBhYcChDhM
1017cdef CUresult cuLaunchCooperativeKernel(CUfunction f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, CUstream hStream, void** kernelParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1018 return _driver._cuLaunchCooperativeKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams)
1021cdef CUresult cuLaunchCooperativeKernelMultiDevice(CUDA_LAUNCH_PARAMS* launchParamsList, unsigned int numDevices, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1022 return _driver._cuLaunchCooperativeKernelMultiDevice(launchParamsList, numDevices, flags)
1025cdef CUresult cuLaunchHostFunc(CUstream hStream, CUhostFn fn, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil:
1026 return _driver._cuLaunchHostFunc(hStream, fn, userData) 2JbKb
1029cdef CUresult cuFuncSetBlockShape(CUfunction hfunc, int x, int y, int z) except ?CUDA_ERROR_NOT_FOUND nogil:
1030 return _driver._cuFuncSetBlockShape(hfunc, x, y, z)
1033cdef CUresult cuFuncSetSharedSize(CUfunction hfunc, unsigned int bytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1034 return _driver._cuFuncSetSharedSize(hfunc, bytes)
1037cdef CUresult cuParamSetSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1038 return _driver._cuParamSetSize(hfunc, numbytes)
1041cdef CUresult cuParamSeti(CUfunction hfunc, int offset, unsigned int value) except ?CUDA_ERROR_NOT_FOUND nogil:
1042 return _driver._cuParamSeti(hfunc, offset, value)
1045cdef CUresult cuParamSetf(CUfunction hfunc, int offset, float value) except ?CUDA_ERROR_NOT_FOUND nogil:
1046 return _driver._cuParamSetf(hfunc, offset, value)
1049cdef CUresult cuParamSetv(CUfunction hfunc, int offset, void* ptr, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1050 return _driver._cuParamSetv(hfunc, offset, ptr, numbytes)
1053cdef CUresult cuLaunch(CUfunction f) except ?CUDA_ERROR_NOT_FOUND nogil:
1054 return _driver._cuLaunch(f)
1057cdef CUresult cuLaunchGrid(CUfunction f, int grid_width, int grid_height) except ?CUDA_ERROR_NOT_FOUND nogil:
1058 return _driver._cuLaunchGrid(f, grid_width, grid_height)
1061cdef CUresult cuLaunchGridAsync(CUfunction f, int grid_width, int grid_height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1062 return _driver._cuLaunchGridAsync(f, grid_width, grid_height, hStream)
1065cdef CUresult cuParamSetTexRef(CUfunction hfunc, int texunit, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1066 return _driver._cuParamSetTexRef(hfunc, texunit, hTexRef)
1069cdef CUresult cuFuncSetSharedMemConfig(CUfunction hfunc, CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil:
1070 return _driver._cuFuncSetSharedMemConfig(hfunc, config)
1073cdef CUresult cuGraphCreate(CUgraph* phGraph, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1074 return _driver._cuGraphCreate(phGraph, flags) 2XyYyZy0y1y2y3y4y5yEl}iFl6y~iGlHl7y8y9y!y#y{i$y%y'y(y2 )y*y+y,y-y.y/y:y;y=y?ySX@y[y]y^y_y`y{y|y}y~yazbzczdzezfzgzhzizIlJl@baj{d|dbjKlLlMlNlod}dIhJhKhLhOlPlQlRl[bcj~daedjSlTlUlVlpdbeMhNhOhPhWlXlYlejZljzfj0l1l2lgj3lhj4l5l6l7l]bijcedejj8l9l!l#lqdeeQhRhShTh$l%l'l(l^bkjfegelj)l*l+l,lrdheUhVhWhXh-l.l/l:l_bmjiejenj;l=l?l@lsdkeYhZh0h1h[l]l^l_l`bojlemepj`l{l|l}ltdne2h3h4h5h~lambmqjcmrjdmemfmsjgmtjhmim_xjmujkmvjlmmmAl(Y)Y*Y+YQx,Y`x=r`k+q;dBlcdmpnpopppCbDbEbFb/b:b'b~ =d@iLbMb?d[iK N agX ^ _ (b;b=iO L A F B 8L]pylzlb Cl=bDlZ 9L`i.r!L/r:r{x|xGh| }x#L-YmnecrqLjMjNjOj*znnonpnHeIe=h+zrnsnunfctqRjSjTjUj.zvnwnxnJeKe?h/zznAnVbLeMeVjvgwgxgDdNe@hygzgOe' PeEd1c2c3c[hFdGdHdWbXb4c]hIdJdjbkbYb, - . / ^hlbBgCgDgEg_hBnCn5cKdFgvqlrDnEngcwqYjZj0j1j:zFnGnHnReSe`h;zJnKn2jZbLn|h}h~haiLt3j4j5jLdMdGgMt7j8j9jmbNdOdbiTeUeVe6cWeHgXeYemr0bNndi!j#jeiNt$j%j'jPdQdIgOt)j*jfigiZe0e1e2ehi3e4e5e6enbRdSd7e8e9eTdJg!e#ePnhczq+j,j-j.jQnRnSn$e%eii]zTnUnKgLgMgNgVnWnXnYnZnjiicOgPgUdVdQg/j'e(e)e*e7c+e:j,e-ejc8c9c!cWdkclcobmcncoc0npcAq;j=j?j@j^z1n2n3n.e/eki_z5n6n3 1b2bqc#c$c%c'c: (c)cXd:e;eYd=e?e[jrclimi@e[eni7nRgSgTg]eZdUg9nVgWg!nsc]j^j_j`j#n$n%n^e_eoi'n(npipb{jYgZg0g1gDqdlqiri*c+c`eEqtiui)n*ntcFq~jakbkck{z+n,n-n{e|evi|z/n:n3b}e~edk2g3g4g0dafwi5g6gbf( cf1d^d,c2dxi3d4d5d4b5b-czi6d7dqbrb6b; = ? @ Aisb7g8g9g!gBi;n=n.c8d#gHq?n@n[nucIqgkhkikjk}z]n^n_nefffCi~z{n|n}nvcJqlkmknkokbA~naobogfhfDicAdoeopktb9d!dEiifjfkf/clf$gmfnfqk7bfoGirkskHiVttkukvk#d$d%gWtxkykIiJiofpfqfrfKisftfufvfub%d'dwfxfyf(d'gzfAfgowcLqzkAkBkCkhoiojoBfCfLifAkolo(g)g*g+gmonooopoqoMixc,g-g)d*d.gDkDfEfFfGf:cHfEkIfJfyc;c=c?c+dzcAcvbBcCcDcroEcMqFkGkHkIkgAsotouoKfLfNihAwoxo4 8b9bFc@c[c]c^c[ _c`c,dMfNf-dOfPfyoGcJkKk/g:gLkNqOiPiQiQfRfRiOqSiTiAoHcMkNkOkPkBoCoDoSfTfUiEoFoViwbQk=g?g@g[gQqWiXiYi{c|cUfRq0i1iHoIoIcSqSkTkUkVkkAJoKoLoVfWf2ilANoOoPoJcVqXkYkZk0knAQoRoSoXfYf3ioAUoVoWoKcXq2k3k4k5krAXoYoZoZf0f4isA1o2o3oLcZq7k8k9k!kvA4o5o6o1f2f5iwA8o9o!oMc1q$k%k'k(kzA#o$o%o3f4f6iAA(o)o*oNc3q*k+k,k-kDA+o,o-o5f6f7iEA/o:o;oOc5q/k:k;k=kGA=o?o@o7f8f8iHA]o^o_oPc6q@k[k]k^kJA`o{o|o9f!f9iKA}o~o
1077cdef CUresult cuGraphAddKernelNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1078 return _driver._cuGraphAddKernelNode_v2(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 22 ybzbAb!bBb$i_k@bod[bpd]bqd^brd_bsd`btd;dCbDbEbFb'bK N agX ^ _ (bO L A F B b Z ecHefcJeVbDd' WbjbkbYb, - . / lb5cgcReZbLdmb6c0bPdnbhc$eic*ejc8c9c!cWdkclcobmcncocpc.e3 : rc]esc^epb*ctc{e3b0d( 4bqbrb6b; = ? @ sb.cucefvcgftb/c7b#dubwcBfxcGfyc;c=c?c+dzcAcvbBcCcDcEcKf4 [ GcQfHcSfwb{cIcVfJcXfKcZfLc1fMc3fNc5fOc7fPc9f
1081cdef CUresult cuGraphKernelNodeGetParams(CUgraphNode hNode, CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1082 return _driver._cuGraphKernelNodeGetParams_v2(hNode, nodeParams) 2$LCbDbEbFb'b(bb
1085cdef CUresult cuGraphKernelNodeSetParams(CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1086 return _driver._cuGraphKernelNodeSetParams_v2(hNode, nodeParams)
1089cdef CUresult cuGraphAddMemcpyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1090 return _driver._cuGraphAddMemcpyNode(phGraphNode, hGraph, dependencies, numDependencies, copyParams, ctx) 26 7 8 * }dbeeehekeneIeKeNeXbKdSeMdWeQdTd%e7cob/e3 1b2bqc#c$c%c'cYdZd_e+c|eaf5b8dffhflf$d(dCf:cvbLf4 8b9bFc@c[c]c^c-dRfTf|cWfYf0f2f4f6f8f!f
1093cdef CUresult cuGraphMemcpyNodeGetParams(CUgraphNode hNode, CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1094 return _driver._cuGraphMemcpyNodeGetParams(hNode, nodeParams) 1|
1097cdef CUresult cuGraphMemcpyNodeSetParams(CUgraphNode hNode, const CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1098 return _driver._cuGraphMemcpyNodeSetParams(hNode, nodeParams)
1101cdef CUresult cuGraphAddMemsetNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1102 return _driver._cuGraphAddMemsetNode(phGraphNode, hGraph, dependencies, numDependencies, memsetParams, ctx) 26 7 8 * #b$b%bQcIhJhKhLhMhNhOhPhQhRhShThUhVhWhXhYhZh0h1h2h3h4h5hb =b=h?h@h4cFg`hGgHgIgJgii+emcki: (c)cXd:e;eYd=e?eUgoi`eviwi-c#gCiDi$g%g'gLiHfBcNi[ _c`c,dMfNf-dOfPfRiUiUf2i3i4i5i6i7i8i9i
1105cdef CUresult cuGraphMemsetNodeGetParams(CUgraphNode hNode, CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1106 return _driver._cuGraphMemsetNodeGetParams(hNode, nodeParams) 1b
1109cdef CUresult cuGraphMemsetNodeSetParams(CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1110 return _driver._cuGraphMemsetNodeSetParams(hNode, nodeParams)
1113cdef CUresult cuGraphAddHostNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1114 return _driver._cuGraphAddHostNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2hdidjdKlLlSlTl8l9l)l*l;l=l`l{l/b:b;bnnvnvgFdYb_hFn3jTe$jgihi7eQnKgLgMgNg'eWd1nqcXdRg#ndl+n2g3d6bBi]n~niftkJiKiwfho(g)g*g+gDf+dsoFc,dOiBoWiJoQoXo4o#o+o=o`o
1117cdef CUresult cuGraphHostNodeGetParams(CUgraphNode hNode, CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1118 return _driver._cuGraphHostNodeGetParams(hNode, nodeParams)
1121cdef CUresult cuGraphHostNodeSetParams(CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1122 return _driver._cuGraphHostNodeSetParams(hNode, nodeParams)
1125cdef CUresult cuGraphAddChildGraphNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1126 return _driver._cuGraphAddChildGraphNode(phGraphNode, hGraph, dependencies, numDependencies, childGraph) 2S 2 @b[b]b^b_b`b'b(becfcVb' jbkbYb, - . / lbgcZbmb0bnbhcicjcpc3 : rcscpbtc3b( qbrb6b; = ? @ sbucvctb7bubwcxcycEc4 [ GcHcwbIcJcKcLcMcNcOcPc
1129cdef CUresult cuGraphChildGraphNodeGetGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1130 return _driver._cuGraphChildGraphNodeGetGraph(hNode, phGraph) 22 @b[b]b^b_b`b'b(becfcVb' jbkbYb, - . / lbgcZbmb0bnbhcicjcpc3 : rcscpbtc3b( qbrb6b; = ? @ sbucvctb7bubwcxcycEc4 [ GcHcwbIcJcKcLcMcNcOcPc
1133cdef CUresult cuGraphAddEmptyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1134 return _driver._cuGraphAddEmptyNode(phGraphNode, hGraph, dependencies, numDependencies) 2}i~i{i6 7 8 * (q)q*qaj}dcjbeejfjgjhjijeekjhemjkeojneqjrjsjtj_xujvj`x`kO L A F B 8L]pylzlClDl`i.r/r:r{x|x}x#LLjIeRjKeNeEdXbBgKdYjSe|hMd9jmbNdOdbiTeUeVe6cWeHgXeYediQdTd+j%ePg7cob;j/e3 1b2bqc#c$c%c'cYdmiZd]j_eYg+c~j|eaf1d5b7g8dgkfflkhfpktb9d!dEiifjfkf/clf$gmfnfGi$d(dzkCf-g:cvbFkLf4 8b9bFc@c[c]c^c-dKkRfMkTf=g|cSkWfXkYf2k0f7k2f$k4f*k6f/k8f@k!f
1137cdef CUresult cuGraphAddEventRecordNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1138 return _driver._cuGraphAddEventRecordNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2.b{d~dcefeiele~ =d@iLbMbX MjSjLe1cjbCgZj}hNd!jfigiZe0e1e2eRd,jUd8c=j1b(c@e^jZgak}e^dqb8ghkmk9drkIiJiofpfqfrf%dAk)d;cGk8b_c/gNk?gTkYk3k8k%k+k:k[k
1141cdef CUresult cuGraphEventRecordNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1142 return _driver._cuGraphEventRecordNodeGetEvent(hNode, event_out)
1145cdef CUresult cuGraphEventRecordNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1146 return _driver._cuGraphEventRecordNodeSetEvent(hNode, event)
1149cdef CUresult cuGraphAddEventWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1150 return _driver._cuGraphAddEventWaitNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2.b|daedegejemeLbMb?d[iNjTjMe2ckbDg0j~hOd#jfihi3e4e5e6eSd-jVd9c?j2b)c[e_j0gbk~e,crb9giknk!dskIiKisftfufvf'dBk*d=cHk9b`c:gOk@gUkZk4k9k'k,k;k]k
1153cdef CUresult cuGraphEventWaitNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1154 return _driver._cuGraphEventWaitNodeGetEvent(hNode, event_out)
1157cdef CUresult cuGraphEventWaitNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1158 return _driver._cuGraphEventWaitNodeSetEvent(hNode, event)
1161cdef CUresult cuGraphAddExternalSemaphoresSignalNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1162 return _driver._cuGraphAddExternalSemaphoresSignalNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
1165cdef CUresult cuGraphExternalSemaphoresSignalNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1166 return _driver._cuGraphExternalSemaphoresSignalNodeGetParams(hNode, params_out)
1169cdef CUresult cuGraphExternalSemaphoresSignalNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1170 return _driver._cuGraphExternalSemaphoresSignalNodeSetParams(hNode, nodeParams)
1173cdef CUresult cuGraphAddExternalSemaphoresWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1174 return _driver._cuGraphAddExternalSemaphoresWaitNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
1177cdef CUresult cuGraphExternalSemaphoresWaitNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_WAIT_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1178 return _driver._cuGraphExternalSemaphoresWaitNodeGetParams(hNode, params_out)
1181cdef CUresult cuGraphExternalSemaphoresWaitNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1182 return _driver._cuGraphExternalSemaphoresWaitNodeSetParams(hNode, nodeParams)
1185cdef CUresult cuGraphAddBatchMemOpNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1186 return _driver._cuGraphAddBatchMemOpNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams)
1189cdef CUresult cuGraphBatchMemOpNodeGetParams(CUgraphNode hNode, CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1190 return _driver._cuGraphBatchMemOpNodeGetParams(hNode, nodeParams_out)
1193cdef CUresult cuGraphBatchMemOpNodeSetParams(CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1194 return _driver._cuGraphBatchMemOpNodeSetParams(hNode, nodeParams)
1197cdef CUresult cuGraphExecBatchMemOpNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1198 return _driver._cuGraphExecBatchMemOpNodeSetParams(hGraphExec, hNode, nodeParams)
1201cdef CUresult cuGraphAddMemAllocNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUDA_MEM_ALLOC_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1202 return _driver._cuGraphAddMemAllocNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2PAQA!q;rMuRANuEl}iFl~iGlHl#q~cadbd:d6 7 8 * #b$b%bQc$q%q'q(q)q*qIlJlaj{d|dbjod}dIhJhKhLhQlRlcj~daedjpdbeMhNhOhPhYlejZlfj0l1l2lgj3lhj4l5l6l7lijcedejjqdeeQhRhShTh'l(lkjfegeljrdheUhVhWhXh/l:lmjiejenjsdkeYhZh0h1h^l_lojlemepjtdne2h3h4h5hbmqjcmrjdmemfmsjgmtjhmimjmujkmvjlmmm`k+qcd=d?dGhmnLjOjIe=hunRjUjKe?hVbLeMeVjvgwgxgDdNe@hygzgOeEd3cXb4c^hBgEgKdFgEnYj1jSe`h2j|haiMdGg9jmbNdOdbiTeUeVe6cWeHgXeYemrdieiQdIgnbRdSd7e8e9eTdJg!e#ePn+j.j%eiijiPgQg7c+e!cobmc0n;j@j/eki3 1b2bqc#c$c%c'c: (c)cXd:e;eYd=e?e[jminiZdUg!n]j`j_eoipiYg1g+c`e*n~jck|evi3b}e~edk2g3g4g0dafwi5g6gbf1d2d5b-cAi7g!g8d#g[ngkjkffCi}nlkokhfDipktb9d!dEiifjfkf/clf$gmfnfqkGiHi$d%gub%d'dwfxfyf(d'gzfAfgozkCkCfLiMi-g.g:cHf?cvbBcroFkIkLfNi4 8b9bFc@c[c]c^c[ _c`c,dMfNf-dOfPfyoKkLkRfRiAoMkPkTfUiVi=g[g|cUfIoSkVkWf2iPoXk0kYf3iWo2k5k0f4i3o7k!k2f5i!o$k(k4f6i*o*k-k6f7i;o/k=k8f8i_o@k^k!f9i
1205cdef CUresult cuGraphMemAllocNodeGetParams(CUgraphNode hNode, CUDA_MEM_ALLOC_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1206 return _driver._cuGraphMemAllocNodeGetParams(hNode, params_out) 2%L'L(L)L*L+L,L-L.L/L:L;L=L?L@L[L]L^L_L`L{L|L}L~xaybycydyeyfygyhyiyjy
1209cdef CUresult cuGraphAddMemFreeNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil:
1210 return _driver._cuGraphAddMemFreeNode(phGraphNode, hGraph, dependencies, numDependencies, dptr) 2!q#q~cadbd:d6 7 8 * #b$b%bQcbjdjjjljnjpj=rGhOjUjVj3cEg1jaibieinbRdSd7e8e9eTdJg!e#e.jQg!c@jni`j1gckdk2d!gjkokEiHiub%d'dwfxfyf(d'gzfAfCk.g?cIkLkPk[gVk0k5k!k(k-k=k^k
1213cdef CUresult cuGraphMemFreeNodeGetParams(CUgraphNode hNode, CUdeviceptr* dptr_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1214 return _driver._cuGraphMemFreeNodeGetParams(hNode, dptr_out)
1217cdef CUresult cuDeviceGraphMemTrim(CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
1218 return _driver._cuDeviceGraphMemTrim(device) 1!#$
1221cdef CUresult cuDeviceGetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1222 return _driver._cuDeviceGetGraphMemAttribute(device, attr, value) 2! # $ X2Gh
1225cdef CUresult cuDeviceSetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1226 return _driver._cuDeviceSetGraphMemAttribute(device, attr, value) 1!#$
1229cdef CUresult cuGraphClone(CUgraph* phGraphClone, CUgraph originalGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1230 return _driver._cuGraphClone(phGraphClone, originalGraph) 2LbN ^
1233cdef CUresult cuGraphNodeFindInClone(CUgraphNode* phNode, CUgraphNode hOriginalNode, CUgraph hClonedGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1234 return _driver._cuGraphNodeFindInClone(phNode, hOriginalNode, hClonedGraph)
1237cdef CUresult cuGraphNodeGetType(CUgraphNode hNode, CUgraphNodeType* type) except ?CUDA_ERROR_NOT_FOUND nogil:
1238 return _driver._cuGraphNodeGetType(hNode, type) 2$L%L'L(L)L*L+L,L-L.L/L:L;L=L?L@L[L]L^L_L`L{L|L}L~xaybycydyeyfy~LgyhyiyjyY2Z202122232425262728292!2#2$2%2'2(2)2CbDbEbFb'b(b=ib
1241cdef CUresult cuGraphGetNodes(CUgraph hGraph, CUgraphNode* nodes, size_t* numNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1242 return _driver._cuGraphGetNodes(hGraph, nodes, numNodes) 2Px{i$L%L'L*2(L)L*L+2,2-2+L,L-L.L/L:L.2/2:2;2=2?2@2[2]2;L=L^2?L@L[L]L_2`2{2|2^L_L`L{L|L}L}2~2a3b3c3d3e3f3`xmpnpopppCbDbEbFb'b(b=iO L A F B b =b
1245cdef CUresult cuGraphGetRootNodes(CUgraph hGraph, CUgraphNode* rootNodes, size_t* numRootNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1246 return _driver._cuGraphGetRootNodes(hGraph, rootNodes, numRootNodes)
1249cdef CUresult cuGraphGetEdges(CUgraph hGraph, CUgraphNode* from_, CUgraphNode* to, CUgraphEdgeData* edgeData, size_t* numEdges) except ?CUDA_ERROR_NOT_FOUND nogil:
1250 return _driver._cuGraphGetEdges_v2(hGraph, from_, to, edgeData, numEdges) 2g3h3i3j3k3l3m3{iO L A F B b =b.r
1253cdef CUresult cuGraphNodeGetDependencies(CUgraphNode hNode, CUgraphNode* dependencies, CUgraphEdgeData* edgeData, size_t* numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1254 return _driver._cuGraphNodeGetDependencies_v2(hNode, dependencies, edgeData, numDependencies) 2!q#q{i(q)q*q$i~xayn3bycydyeyo3p3q3r3fy~Lgyhyiyjys3t3u3v3w3x3y3z3`kX F ylzlb .r:r
1257cdef CUresult cuGraphNodeGetDependentNodes(CUgraphNode hNode, CUgraphNode* dependentNodes, CUgraphEdgeData* edgeData, size_t* numDependentNodes) except ?CUDA_ERROR_NOT_FOUND nogil:
1258 return _driver._cuGraphNodeGetDependentNodes_v2(hNode, dependentNodes, edgeData, numDependentNodes) 2{i~xaybycydyeyfy~LgyhyiyjyA3B3C3D3E3F3A B ]pylzlb ClDl:r
1261cdef CUresult cuGraphAddDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1262 return _driver._cuGraphAddDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 2{iA F B ]pylzlb Cl=bDl
1265cdef CUresult cuGraphRemoveDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil:
1266 return _driver._cuGraphRemoveDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 2B ]pylzlb
1269cdef CUresult cuGraphDestroyNode(CUgraphNode hNode) except ?CUDA_ERROR_NOT_FOUND nogil:
1270 return _driver._cuGraphDestroyNode(hNode) 2_xL A F =b#L
1273cdef CUresult cuGraphInstantiate(CUgraphExec* phGraphExec, CUgraph hGraph, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1274 return _driver._cuGraphInstantiateWithFlags(phGraphExec, hGraph, flags) 2LbN ^ `iGh| }x
1277cdef CUresult cuGraphInstantiateWithParams(CUgraphExec* phGraphExec, CUgraph hGraph, CUDA_GRAPH_INSTANTIATE_PARAMS* instantiateParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1278 return _driver._cuGraphInstantiateWithParams(phGraphExec, hGraph, instantiateParams) 2JbKbcgS T 5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J hd~cadbd:d2 .bidjdybzbAb!bBb6 7 8 * #b$b%bQc.Y/Y:Y$q%q'q;dcd/b:bMbK X _ ;bO L A F B b +b,b-bkdldmdx y z C D w P Q R NbObPb! # $ E Y Z Gb)b*bSc
1281cdef CUresult cuGraphExecGetFlags(CUgraphExec hGraphExec, cuuint64_t* flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1282 return _driver._cuGraphExecGetFlags(hGraphExec, flags)
1285cdef CUresult cuGraphExecKernelNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1286 return _driver._cuGraphExecKernelNodeSetParams_v2(hGraphExec, hNode, nodeParams)
1289cdef CUresult cuGraphExecMemcpyNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1290 return _driver._cuGraphExecMemcpyNodeSetParams(hGraphExec, hNode, copyParams, ctx)
1293cdef CUresult cuGraphExecMemsetNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1294 return _driver._cuGraphExecMemsetNodeSetParams(hGraphExec, hNode, memsetParams, ctx)
1297cdef CUresult cuGraphExecHostNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1298 return _driver._cuGraphExecHostNodeSetParams(hGraphExec, hNode, nodeParams)
1301cdef CUresult cuGraphExecChildGraphNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1302 return _driver._cuGraphExecChildGraphNodeSetParams(hGraphExec, hNode, childGraph)
1305cdef CUresult cuGraphExecEventRecordNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1306 return _driver._cuGraphExecEventRecordNodeSetEvent(hGraphExec, hNode, event)
1309cdef CUresult cuGraphExecEventWaitNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil:
1310 return _driver._cuGraphExecEventWaitNodeSetEvent(hGraphExec, hNode, event)
1313cdef CUresult cuGraphExecExternalSemaphoresSignalNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1314 return _driver._cuGraphExecExternalSemaphoresSignalNodeSetParams(hGraphExec, hNode, nodeParams)
1317cdef CUresult cuGraphExecExternalSemaphoresWaitNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1318 return _driver._cuGraphExecExternalSemaphoresWaitNodeSetParams(hGraphExec, hNode, nodeParams)
1321cdef CUresult cuGraphNodeSetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1322 return _driver._cuGraphNodeSetEnabled(hGraphExec, hNode, isEnabled)
1325cdef CUresult cuGraphNodeGetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int* isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil:
1326 return _driver._cuGraphNodeGetEnabled(hGraphExec, hNode, isEnabled)
1329cdef CUresult cuGraphUpload(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1330 return _driver._cuGraphUpload(hGraphExec, hStream) 2T ) hd~cadbd2 .bidjdybzbAbBb6 7 8 #b$b%b/b:b;bx y z C D w P Q R NbObPb! # $
1333cdef CUresult cuGraphLaunch(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1334 return _driver._cuGraphLaunch(hGraphExec, hStream) 2JbKbS T 1 ) c d e f g h i j k l m n o p q r s t u v G H I J hd~cadbd:d2 .bidjdybzbAb!bBb6 7 8 * #b$b%bQccd/b:bLbMbK N X ^ _ ;bO L A F B b x y z C D w P Q R NbObPb! # $ E Y Z Gh|
1337cdef CUresult cuGraphExecDestroy(CUgraphExec hGraphExec) except ?CUDA_ERROR_NOT_FOUND nogil:
1338 return _driver._cuGraphExecDestroy(hGraphExec) 2JbKbcgS T 5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J hd~cadbd:d2 .bidjdybzbAb!bBb6 7 8 * #b$b%bQc.Y/Y:Y$q%q'q;dcd/b:bMbK X _ ;bO L A F B b +b,b-bkdldmdx y z C D w P Q R NbObPb! # $ E Y Z Gb)b*bSc`i| }x
1341cdef CUresult cuGraphDestroy(CUgraph hGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1342 return _driver._cuGraphDestroy(hGraph) 2JbKbcgS T ?i5 1 ) xbc d e f g h i j k l m n o p q r s t u v G H I J HCICJCKCLCMCNCOCPCQCRCSCTCUCVCWCXCYCZC0C1C{i2C3C4C5C2 6C#u7C8C9C!C#C$C%C'C(C)C*C+C,C-C.C/C:C;C=C?C@C[C]C^C_C`C{C|C@b}C$u%u~CaDbDcDdDeDfDgDhDiDjDkDlDmD[bnD'u(uoDpDqDrDsDtDuDvDwDxDyDzDADBDCDDDEDFDGDHDIDJDKDLDMDNDOD]bPDQD)u*uRDSDTDUDVDWDXDYDZD0D1D2D3D4D5D^b6D7D+u,u8D9D!D#D$D%D'D(D)D*D+D,D-D.D/D_b:D;D-u.u=D?D@D[D]D^D_D`D{D|D}D~DaEbEcE`bdEeE/u:ufEgEhEiEjEkElEmEnEoEpEqErEsEtEuEvEwExEyEzEAEBECEDE_xEEFEGEHEIEJEAl(Y)Y*Y+YQx,Y`x=r`k+q;dBlcdmpnpopppCbDbEbFb/b:b'b~ =d@iLbMb?d[iK N agX ^ _ (b;b=iO L A F B 8L]pylzlb Cl=bDl+b,b-bkdldmdx y z C D w P Q R NbObPb! # $ E Y Z Gb)b*bddScU 7q`i.r!L/r:r{x|xGh| -Y5Eec7E8E9E;u=u#E$E%E'E(E)E*E+E,E.E/E=Efc@E[E]E?u@u_E`E{E|E}E~EaFbFcFeFfFVbgF[u]uhFiFjFkFlFmFnFoFpF^u' _u`u{ubrcr|u}u~uavbvcvdvevfvgvhvjbivkbjvYbtF, uF- vF. wF/ xFyFlbzFAFkvlvBFCFDFEFFFGFHFIFJFKFLFgcNFOFPFmvnvQFRFSFTFUFVFWFXFYFZF0F1FZb3F4F5Fovpv7F8F9F!F#F$F%F'F(F*F+F,Fmb-Fqvrv.F/F:F;F=F?F@F[F]Fsv0buvvvwvxvyvzvAvBvCvDvEvFvGvHvIvJvKvLvMvNvOvPvQvRvSvTvUvnb|FVvWv}F~FaGbGcGdGeGfGhcgGhGiGXvYvjGkGlGmGnGoGpGqGrGsGtGuGvGwGxGyGzGAGBGCGicDGEGFGZv0vGGHGIGJGKGLGMGNGOGPGQGjcRG1v2vSGTGUGVGWGXGYGZG0Gpc1G2G3G3v4v4G5G6G7G8G9G!G#G$G%G'G3 (G5v6v)G*G+G,G-G: .G7v8v/G:G;G=G?G@G[Grc]G^G_G9v!v`G{G|G}G~GaHbHcHdHeHfHgHschHiH#v$vjHkHlHmHnHoHpHqHrH%vpb(v)v*vdrer,v-v.v/v:v;v=v?v@v[v]vwHxHtczHAHBH^v_vDHEHFHGHHHIHJHKHLHNHOH3bPH`v{vQHRHSHTHUHVHWHXHYH|v( }v~vawfrgrbwcwdwewfwgwhwiwjwkwlwqbmwrbnw6b2H; 3H= 4H? 5H@ 6H7Hsb8H9Howpw!H#H$H%H'H(H)H*H+H,H-Huc/H:H;Hqwrw=H?H@H[H]H^H_H`H{H|H}H~HvcbIcIdIswtwfIgIhIiIjIkIlImInIpIqIrItbsIuwvwtIuIvIwIxIyIzIAIBIww7bywzwAwBwCwDwEwFwGwHwIwJwKwLwMwNwOwPwQwRwSwTwUwVwWwXwYwubGIZw0wHIIIJIKILIMINIOIwcPIQIRI1w2wSITIUIVIWIXIYIZI0I1I2I3I4I5I6I7I8I9I!I#Ixc$I%I'I3w4w(I)I*I+I,I-I.I/I:I;I=Iyc?I5w6w@I[I]I^I_I`I{I|I}IEc~IaJbJ7w8wcJdJeJfJgJhJiJjJkJlJmJ4 nJ9w!woJpJqJrJsJ[ tJ#w$wuJvJwJxJyJzJAJGcBJCJDJ%w'wEJFJGJHJIJJJKJLJMJNJOJPJHcQJRJ(w)wSJTJUJVJWJXJYJZJ0J*wwb,w-w.whrir:w;w=w?w@w[w]w^w_w`w{w5J6JIc8J9J!J|w}w$J%J'J(J)J*J+J,J-J/J:J;JJc?J@J[J~wax^J_J`J{J|J}J~JaKbKdKeKfKKchKiKjKbxcxlKmKnKoKpKqKrKsKtKvKwKxKLczKAKBKdxexDKEKFKGKHKIKJKKKLKNKOKPKMcRKSKTKfxgxVKWKXKYKZK0K1K2K3K5K6K7KNc9K!K#Khxix%K'K(K)K*K+K,K-K.K:K;K=KOc@K[K]Kjxkx_K`K{K|K}K~KaLbLcLeLfLgLPciLjLkLlxmxmLnLoLpLqLrLsLtLuLwLxL
1345cdef CUresult cuGraphExecUpdate(CUgraphExec hGraphExec, CUgraph hGraph, CUgraphExecUpdateResultInfo* resultInfo) except ?CUDA_ERROR_NOT_FOUND nogil:
1346 return _driver._cuGraphExecUpdate_v2(hGraphExec, hGraph, resultInfo) 2E Y Z Gb
1349cdef CUresult cuGraphKernelNodeCopyAttributes(CUgraphNode dst, CUgraphNode src) except ?CUDA_ERROR_NOT_FOUND nogil:
1350 return _driver._cuGraphKernelNodeCopyAttributes(dst, src)
1353cdef CUresult cuGraphKernelNodeGetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, CUkernelNodeAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1354 return _driver._cuGraphKernelNodeGetAttribute(hNode, attr, value_out)
1357cdef CUresult cuGraphKernelNodeSetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, const CUkernelNodeAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil:
1358 return _driver._cuGraphKernelNodeSetAttribute(hNode, attr, value)
1361cdef CUresult cuGraphDebugDotPrint(CUgraph hGraph, const char* path, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1362 return _driver._cuGraphDebugDotPrint(hGraph, path, flags) 2MuNuU
1365cdef CUresult cuUserObjectCreate(CUuserObject* object_out, void* ptr, CUhostFn destroy, unsigned int initialRefcount, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1366 return _driver._cuUserObjectCreate(object_out, ptr, destroy, initialRefcount, flags) 2JbKbhd2 .bidjdybzbAb!bBb$i_k@b{d|dKlLlod[b~daeSlTlpd]bcede8l9lqd^bfege)l*lrd_bieje;l=lsd`bleme`l{ltd;dCbDbEbFb/b:b'b~ =d@iLbMb?d[iK N agX ^ _ (b;bO L A F B b Z ecMjNjnnHefcSjTjvnJeVbLeMevgDd' 1c2cFdWbjbkbYb, - . / lbCgDg_h5cgcZj0jFnReZb}h~h3jLdmbNdOdTe6c0b!j#j$jPdfigiZe0e1e2ehi3e4e5e6enbRdSd7ehc,j-jQn$eKgLgMgNgicUdVd'e*ejc8c9c!cWdkclcobmcncocpc=j?j1n.e3 1b2bqc: (c)cXdrc@e[eRg]esc^j_j#n^epbZg0gdl*ctcakbk+n{e3b}e~e2g0d( ^d,c3d4bqbrb6b; = ? @ sb8g9gBi.cuchkik]nefvcmknk~ngftb9d!dif/c7brksktk#dIiJiofpfqfrfKisftfufvfub%d'dwfwcAkBkhoBf(g)g*g+gxc)d*dDfGfyc;c=c?c+dzcAcvbBcCcDcEcGkHksoKf4 8b9bFc[ _c`c,dGc/g:gOiQfHcNkOkBoSfwb?g@gWi{cIcTkUkJoVfJcYkZkQoXfKc3k4kXoZfLc8k9k4o1fMc%k'k#o3fNc+k,k+o5fOc:k;k=o7fPc[k]k`o9f
1369cdef CUresult cuUserObjectRetain(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1370 return _driver._cuUserObjectRetain(object, count)
1373cdef CUresult cuUserObjectRelease(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1374 return _driver._cuUserObjectRelease(object, count)
1377cdef CUresult cuGraphRetainUserObject(CUgraph graph, CUuserObject object, unsigned int count, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1378 return _driver._cuGraphRetainUserObject(graph, object, count, flags) 2JbKbhd2 .bidjdybzbAb!bBb$i_k@b{d|dKlLlod[b~daeSlTlpd]bcede8l9lqd^bfege)l*lrd_bieje;l=lsd`bleme`l{ltd;dCbDbEbFb/b:b'b~ =d@iLbMb?d[iK N agX ^ _ (b;bO L A F B b Z ecMjNjnnHefcSjTjvnJeVbLeMevgDd' 1c2cFdWbjbkbYb, - . / lbCgDg_h5cgcZj0jFnReZb}h~h3jLdmbNdOdTe6c0b!j#j$jPdfigiZe0e1e2ehi3e4e5e6enbRdSd7ehc,j-jQn$eKgLgMgNgicUdVd'e*ejc8c9c!cWdkclcobmcncocpc=j?j1n.e3 1b2bqc: (c)cXdrc@e[eRg]esc^j_j#n^epbZg0gdl*ctcakbk+n{e3b}e~e2g0d( ^d,c3d4bqbrb6b; = ? @ sb8g9gBi.cuchkik]nefvcmknk~ngftb9d!dif/c7brksktk#dIiJiofpfqfrfKisftfufvfub%d'dwfwcAkBkhoBf(g)g*g+gxc)d*dDfGfyc;c=c?c+dzcAcvbBcCcDcEcGkHksoKf4 8b9bFc[ _c`c,dGc/g:gOiQfHcNkOkBoSfwb?g@gWi{cIcTkUkJoVfJcYkZkQoXfKc3k4kXoZfLc8k9k4o1fMc%k'k#o3fNc+k,k+o5fOc:k;k=o7fPc[k]k`o9f
1381cdef CUresult cuGraphReleaseUserObject(CUgraph graph, CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil:
1382 return _driver._cuGraphReleaseUserObject(graph, object, count)
1385cdef CUresult cuGraphAddNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1386 return _driver._cuGraphAddNode_v2(phGraphNode, hGraph, dependencies, dependencyData, numDependencies, nodeParams) 2c d e f g h i j k l m n o p q r s t u v G H I J PxMlNlOlPlUlVlWlXl!l#l$l%l+l,l-l.l?l@l[l]l|l}l~lamAlBlmpnpopppCbDbEbFb=iE U 9L/r| onpnrnsnwnxnznAnwgxgygzgGdHdIdJd, - . / BnCnlrDnGnHnJnKn4j5j7j8jUeVeXeYe%j'j)j*jZe0e1e2e3e4e5e6e8e9e!e#eRnSnTnUnKgLgMgNgVnWnXnYnZn(e)e,e-ekclcncoc2n3n5n6n#c$c%c'c:e;e=e?eSgTgVgWg$n%n'n(nqiritiui)n,n-n/n:n3g4g5g6g4d5d6d7d; = ? @ ;n=n?n@n^n_n{n|naobodoeojfkfmfnfukvkxkykofpfqfrfsftfufvfxfyfzfAfiojokolo(g)g*g+gmonooopoqoEfFfIfJfzcAcCcDctouowoxo@c[c]c^cMfNfOfPfPiQiSiTiCoDoEoFoXiYi0i1iHoKoLoNoOoRoSoUoVoYoZo1o2o5o6o8o9o$o%o(o)o,o-o/o:o?o@o]o^o{o|o}o~o
1389cdef CUresult cuGraphNodeSetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1390 return _driver._cuGraphNodeSetParams(hNode, nodeParams) 1|
1393cdef CUresult cuGraphExecNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1394 return _driver._cuGraphExecNodeSetParams(hGraphExec, hNode, nodeParams) 1|
1397cdef CUresult cuGraphConditionalHandleCreate(CUgraphConditionalHandle* pHandle_out, CUgraph hGraph, CUcontext ctx, unsigned int defaultLaunchValue, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1398 return _driver._cuGraphConditionalHandleCreate(pHandle_out, hGraph, ctx, defaultLaunchValue, flags) 2c d e f g h i j k l m n o p q r s t u v G H I J PxMlNlOlPlUlVlWlXl!l#l$l%l+l,l-l.l?l@l[l]l|l}l~lamAlQxBlmpnpopppCbDbEbFb=iE U 9LrqonpnrnsntqwnxnznAnwgxgygzgPeGdHdIdJd, - . / ^hlbBgCgDgEg_hBnCn5cKdFgvqlrDnwqGnHnJnKnLn4j5j7j8jUeVeXeYeNn%j'j)j*jZe0e1e2e3e4e5e6e8e9e!e#ezqRnSnTnUnKgLgMgNgVnWnXnYnZnOg(e)e,e-ekclcncocAq2n3n5n6n#c$c%c'c:e;e=e?eliSgTgVgWg$n%n'n(n{jqiritiui)nFq,n-n/n:n3g4g5g6gcf4d5d6d7d; = ? @ Aisb7g8g9g!gBi;n=n.c8d#gHq?n@nIq^n_n{n|nJqaobodoeojfkfmfnffoukvkxkykofpfqfrfsftfufvfxfyfzfAfLqiojokolo(g)g*g+gmonooopoqo,gEfFfIfJfzcAcCcDcMqtouowoxo@c[c]c^cMfNfOfPfJkPiQiSiTiCoDoEoFoQkXiYi0i1iHoSqKoLoNoOoVqRoSoUoVoXqYoZo1o2oZq5o6o8o9o1q$o%o(o)o3q,o-o/o:o5q?o@o]o^o6q{o|o}o~o
1401cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize) except ?CUDA_ERROR_NOT_FOUND nogil:
1402 return _driver._cuOccupancyMaxActiveBlocksPerMultiprocessor(numBlocks, func, blockSize, dynamicSMemSize) 2]dSuTuUuVuWuXuYuZu0u1u2u3u4u5u6u7u8u9u
1405cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1406 return _driver._cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(numBlocks, func, blockSize, dynamicSMemSize, flags)
1409cdef CUresult cuOccupancyMaxPotentialBlockSize(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit) except ?CUDA_ERROR_NOT_FOUND nogil:
1410 return _driver._cuOccupancyMaxPotentialBlockSize(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit) 2kClCmCnCoCpCqCrCsCtCuCvCwCxCyCzCACBCCCDCEC
1413cdef CUresult cuOccupancyMaxPotentialBlockSizeWithFlags(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1414 return _driver._cuOccupancyMaxPotentialBlockSizeWithFlags(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit, flags)
1417cdef CUresult cuOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, CUfunction func, int numBlocks, int blockSize) except ?CUDA_ERROR_NOT_FOUND nogil:
1418 return _driver._cuOccupancyAvailableDynamicSMemPerBlock(dynamicSmemSize, func, numBlocks, blockSize) 2eCfCgChCiCjC
1421cdef CUresult cuOccupancyMaxPotentialClusterSize(int* clusterSize, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1422 return _driver._cuOccupancyMaxPotentialClusterSize(clusterSize, func, config)
1425cdef CUresult cuOccupancyMaxActiveClusters(int* numClusters, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil:
1426 return _driver._cuOccupancyMaxActiveClusters(numClusters, func, config)
1429cdef CUresult cuTexRefSetArray(CUtexref hTexRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1430 return _driver._cuTexRefSetArray(hTexRef, hArray, Flags)
1433cdef CUresult cuTexRefSetMipmappedArray(CUtexref hTexRef, CUmipmappedArray hMipmappedArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1434 return _driver._cuTexRefSetMipmappedArray(hTexRef, hMipmappedArray, Flags)
1437cdef CUresult cuTexRefSetAddress(size_t* ByteOffset, CUtexref hTexRef, CUdeviceptr dptr, size_t bytes) except ?CUDA_ERROR_NOT_FOUND nogil:
1438 return _driver._cuTexRefSetAddress_v2(ByteOffset, hTexRef, dptr, bytes)
1441cdef CUresult cuTexRefSetAddress2D(CUtexref hTexRef, const CUDA_ARRAY_DESCRIPTOR* desc, CUdeviceptr dptr, size_t Pitch) except ?CUDA_ERROR_NOT_FOUND nogil:
1442 return _driver._cuTexRefSetAddress2D_v3(hTexRef, desc, dptr, Pitch)
1445cdef CUresult cuTexRefSetFormat(CUtexref hTexRef, CUarray_format fmt, int NumPackedComponents) except ?CUDA_ERROR_NOT_FOUND nogil:
1446 return _driver._cuTexRefSetFormat(hTexRef, fmt, NumPackedComponents)
1449cdef CUresult cuTexRefSetAddressMode(CUtexref hTexRef, int dim, CUaddress_mode am) except ?CUDA_ERROR_NOT_FOUND nogil:
1450 return _driver._cuTexRefSetAddressMode(hTexRef, dim, am)
1453cdef CUresult cuTexRefSetFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1454 return _driver._cuTexRefSetFilterMode(hTexRef, fm)
1457cdef CUresult cuTexRefSetMipmapFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil:
1458 return _driver._cuTexRefSetMipmapFilterMode(hTexRef, fm)
1461cdef CUresult cuTexRefSetMipmapLevelBias(CUtexref hTexRef, float bias) except ?CUDA_ERROR_NOT_FOUND nogil:
1462 return _driver._cuTexRefSetMipmapLevelBias(hTexRef, bias)
1465cdef CUresult cuTexRefSetMipmapLevelClamp(CUtexref hTexRef, float minMipmapLevelClamp, float maxMipmapLevelClamp) except ?CUDA_ERROR_NOT_FOUND nogil:
1466 return _driver._cuTexRefSetMipmapLevelClamp(hTexRef, minMipmapLevelClamp, maxMipmapLevelClamp)
1469cdef CUresult cuTexRefSetMaxAnisotropy(CUtexref hTexRef, unsigned int maxAniso) except ?CUDA_ERROR_NOT_FOUND nogil:
1470 return _driver._cuTexRefSetMaxAnisotropy(hTexRef, maxAniso)
1473cdef CUresult cuTexRefSetBorderColor(CUtexref hTexRef, float* pBorderColor) except ?CUDA_ERROR_NOT_FOUND nogil:
1474 return _driver._cuTexRefSetBorderColor(hTexRef, pBorderColor)
1477cdef CUresult cuTexRefSetFlags(CUtexref hTexRef, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1478 return _driver._cuTexRefSetFlags(hTexRef, Flags)
1481cdef CUresult cuTexRefGetAddress(CUdeviceptr* pdptr, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1482 return _driver._cuTexRefGetAddress_v2(pdptr, hTexRef)
1485cdef CUresult cuTexRefGetArray(CUarray* phArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1486 return _driver._cuTexRefGetArray(phArray, hTexRef)
1489cdef CUresult cuTexRefGetMipmappedArray(CUmipmappedArray* phMipmappedArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1490 return _driver._cuTexRefGetMipmappedArray(phMipmappedArray, hTexRef)
1493cdef CUresult cuTexRefGetAddressMode(CUaddress_mode* pam, CUtexref hTexRef, int dim) except ?CUDA_ERROR_NOT_FOUND nogil:
1494 return _driver._cuTexRefGetAddressMode(pam, hTexRef, dim)
1497cdef CUresult cuTexRefGetFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1498 return _driver._cuTexRefGetFilterMode(pfm, hTexRef)
1501cdef CUresult cuTexRefGetFormat(CUarray_format* pFormat, int* pNumChannels, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1502 return _driver._cuTexRefGetFormat(pFormat, pNumChannels, hTexRef)
1505cdef CUresult cuTexRefGetMipmapFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1506 return _driver._cuTexRefGetMipmapFilterMode(pfm, hTexRef)
1509cdef CUresult cuTexRefGetMipmapLevelBias(float* pbias, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1510 return _driver._cuTexRefGetMipmapLevelBias(pbias, hTexRef)
1513cdef CUresult cuTexRefGetMipmapLevelClamp(float* pminMipmapLevelClamp, float* pmaxMipmapLevelClamp, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1514 return _driver._cuTexRefGetMipmapLevelClamp(pminMipmapLevelClamp, pmaxMipmapLevelClamp, hTexRef)
1517cdef CUresult cuTexRefGetMaxAnisotropy(int* pmaxAniso, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1518 return _driver._cuTexRefGetMaxAnisotropy(pmaxAniso, hTexRef)
1521cdef CUresult cuTexRefGetBorderColor(float* pBorderColor, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1522 return _driver._cuTexRefGetBorderColor(pBorderColor, hTexRef)
1525cdef CUresult cuTexRefGetFlags(unsigned int* pFlags, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1526 return _driver._cuTexRefGetFlags(pFlags, hTexRef)
1529cdef CUresult cuTexRefCreate(CUtexref* pTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1530 return _driver._cuTexRefCreate(pTexRef)
1533cdef CUresult cuTexRefDestroy(CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1534 return _driver._cuTexRefDestroy(hTexRef)
1537cdef CUresult cuSurfRefSetArray(CUsurfref hSurfRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1538 return _driver._cuSurfRefSetArray(hSurfRef, hArray, Flags)
1541cdef CUresult cuSurfRefGetArray(CUarray* phArray, CUsurfref hSurfRef) except ?CUDA_ERROR_NOT_FOUND nogil:
1542 return _driver._cuSurfRefGetArray(phArray, hSurfRef)
1545cdef CUresult cuTexObjectCreate(CUtexObject* pTexObject, const CUDA_RESOURCE_DESC* pResDesc, const CUDA_TEXTURE_DESC* pTexDesc, const CUDA_RESOURCE_VIEW_DESC* pResViewDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
1546 return _driver._cuTexObjectCreate(pTexObject, pResDesc, pTexDesc, pResViewDesc)
1549cdef CUresult cuTexObjectDestroy(CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1550 return _driver._cuTexObjectDestroy(texObject)
1553cdef CUresult cuTexObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1554 return _driver._cuTexObjectGetResourceDesc(pResDesc, texObject)
1557cdef CUresult cuTexObjectGetTextureDesc(CUDA_TEXTURE_DESC* pTexDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1558 return _driver._cuTexObjectGetTextureDesc(pTexDesc, texObject)
1561cdef CUresult cuTexObjectGetResourceViewDesc(CUDA_RESOURCE_VIEW_DESC* pResViewDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1562 return _driver._cuTexObjectGetResourceViewDesc(pResViewDesc, texObject)
1565cdef CUresult cuSurfObjectCreate(CUsurfObject* pSurfObject, const CUDA_RESOURCE_DESC* pResDesc) except ?CUDA_ERROR_NOT_FOUND nogil:
1566 return _driver._cuSurfObjectCreate(pSurfObject, pResDesc)
1569cdef CUresult cuSurfObjectDestroy(CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1570 return _driver._cuSurfObjectDestroy(surfObject)
1573cdef CUresult cuSurfObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil:
1574 return _driver._cuSurfObjectGetResourceDesc(pResDesc, surfObject)
1577cdef CUresult cuTensorMapEncodeTiled(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, const cuuint32_t* boxDim, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil:
1578 return _driver._cuTensorMapEncodeTiled(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, boxDim, elementStrides, interleave, swizzle, l2Promotion, oobFill)
1581cdef CUresult cuTensorMapEncodeIm2col(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, const int* pixelBoxLowerCorner, const int* pixelBoxUpperCorner, cuuint32_t channelsPerPixel, cuuint32_t pixelsPerColumn, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil:
1582 return _driver._cuTensorMapEncodeIm2col(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCorner, pixelBoxUpperCorner, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, swizzle, l2Promotion, oobFill)
1585cdef CUresult cuTensorMapEncodeIm2colWide(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, int pixelBoxLowerCornerWidth, int pixelBoxUpperCornerWidth, cuuint32_t channelsPerPixel, cuuint32_t pixelsPerColumn, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapIm2ColWideMode mode, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil:
1586 return _driver._cuTensorMapEncodeIm2colWide(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCornerWidth, pixelBoxUpperCornerWidth, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, mode, swizzle, l2Promotion, oobFill)
1589cdef CUresult cuTensorMapReplaceAddress(CUtensorMap* tensorMap, void* globalAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1590 return _driver._cuTensorMapReplaceAddress(tensorMap, globalAddress)
1593cdef CUresult cuDeviceCanAccessPeer(int* canAccessPeer, CUdevice dev, CUdevice peerDev) except ?CUDA_ERROR_NOT_FOUND nogil:
1594 return _driver._cuDeviceCanAccessPeer(canAccessPeer, dev, peerDev)
1597cdef CUresult cuCtxEnablePeerAccess(CUcontext peerContext, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1598 return _driver._cuCtxEnablePeerAccess(peerContext, Flags)
1601cdef CUresult cuCtxDisablePeerAccess(CUcontext peerContext) except ?CUDA_ERROR_NOT_FOUND nogil:
1602 return _driver._cuCtxDisablePeerAccess(peerContext)
1605cdef CUresult cuDeviceGetP2PAttribute(int* value, CUdevice_P2PAttribute attrib, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil:
1606 return _driver._cuDeviceGetP2PAttribute(value, attrib, srcDevice, dstDevice)
1609cdef CUresult cuGraphicsUnregisterResource(CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1610 return _driver._cuGraphicsUnregisterResource(resource) 2]g`g{g|gkp;Y=Y?Y@Y[Y]Y}g~gahjg^Ybhch_Ydh`Y{Y|Y}Y
1613cdef CUresult cuGraphicsSubResourceGetMappedArray(CUarray* pArray, CUgraphicsResource resource, unsigned int arrayIndex, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil:
1614 return _driver._cuGraphicsSubResourceGetMappedArray(pArray, resource, arrayIndex, mipLevel)
1617cdef CUresult cuGraphicsResourceGetMappedMipmappedArray(CUmipmappedArray* pMipmappedArray, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1618 return _driver._cuGraphicsResourceGetMappedMipmappedArray(pMipmappedArray, resource)
1621cdef CUresult cuGraphicsResourceGetMappedPointer(CUdeviceptr* pDevPtr, size_t* pSize, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil:
1622 return _driver._cuGraphicsResourceGetMappedPointer_v2(pDevPtr, pSize, resource) 2`gjp{g|g}g~gahjgbhchdhal
1625cdef CUresult cuGraphicsResourceSetMapFlags(CUgraphicsResource resource, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1626 return _driver._cuGraphicsResourceSetMapFlags_v2(resource, flags)
1629cdef CUresult cuGraphicsMapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1630 return _driver._cuGraphicsMapResources(count, resources, hStream) 2`gjp{g|g}g~gahjgbhchdhal
1633cdef CUresult cuGraphicsUnmapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1634 return _driver._cuGraphicsUnmapResources(count, resources, hStream) 2]g`g{g|g}g~gahjgbhchdhal
1637cdef CUresult cuGetProcAddress(const char* symbol, void** pfn, int cudaVersion, cuuint64_t flags, CUdriverProcAddressQueryResult* symbolStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
1638 return _driver._cuGetProcAddress_v2(symbol, pfn, cudaVersion, flags, symbolStatus)
1641cdef CUresult cuCoredumpGetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1642 return _driver._cuCoredumpGetAttribute(attrib, value, size)
1645cdef CUresult cuCoredumpGetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1646 return _driver._cuCoredumpGetAttributeGlobal(attrib, value, size) 2~Y
1649cdef CUresult cuCoredumpSetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1650 return _driver._cuCoredumpSetAttribute(attrib, value, size)
1653cdef CUresult cuCoredumpSetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil:
1654 return _driver._cuCoredumpSetAttributeGlobal(attrib, value, size) 2~Y
1657cdef CUresult cuGetExportTable(const void** ppExportTable, const CUuuid* pExportTableId) except ?CUDA_ERROR_NOT_FOUND nogil:
1658 return _driver._cuGetExportTable(ppExportTable, pExportTableId)
1661cdef CUresult cuGreenCtxCreate(CUgreenCtx* phCtx, CUdevResourceDesc desc, CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1662 return _driver._cuGreenCtxCreate(phCtx, desc, dev, flags) 2elBjCjteV W DjEjFjGjHjIj
1665cdef CUresult cuGreenCtxDestroy(CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1666 return _driver._cuGreenCtxDestroy(hCtx) 2elWEXEYEV W ZE0E1E2E3E4E
1669cdef CUresult cuCtxFromGreenCtx(CUcontext* pContext, CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1670 return _driver._cuCtxFromGreenCtx(pContext, hCtx) 2elBjCjteV W DjEjFjGjHjIj
1673cdef CUresult cuDeviceGetDevResource(CUdevice device, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1674 return _driver._cuDeviceGetDevResource(device, resource, type) 2aZbZTzBjCjtetmumDjEjFjGjHjIjUzVzWzXzYzZz0z1z2z3z4z5z6z7z8z9z!z#z
1677cdef CUresult cuCtxGetDevResource(CUcontext hCtx, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1678 return _driver._cuCtxGetDevResource(hCtx, resource, type)
1681cdef CUresult cuGreenCtxGetDevResource(CUgreenCtx hCtx, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1682 return _driver._cuGreenCtxGetDevResource(hCtx, resource, type) 2elG3)x
1685cdef CUresult cuDevSmResourceSplitByCount(CUdevResource* result, unsigned int* nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, unsigned int minCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1686 return _driver._cuDevSmResourceSplitByCount(result, nbGroups, input, remainder, flags, minCount) 2bZ
1689cdef CUresult cuDevResourceGenerateDesc(CUdevResourceDesc* phDesc, CUdevResource* resources, unsigned int nbResources) except ?CUDA_ERROR_NOT_FOUND nogil:
1690 return _driver._cuDevResourceGenerateDesc(phDesc, resources, nbResources) 2elBjCjteV W DjEjFjGjHjIj
1693cdef CUresult cuGreenCtxRecordEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1694 return _driver._cuGreenCtxRecordEvent(hCtx, hEvent)
1697cdef CUresult cuGreenCtxWaitEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil:
1698 return _driver._cuGreenCtxWaitEvent(hCtx, hEvent)
1701cdef CUresult cuStreamGetGreenCtx(CUstream hStream, CUgreenCtx* phCtx) except ?CUDA_ERROR_NOT_FOUND nogil:
1702 return _driver._cuStreamGetGreenCtx(hStream, phCtx)
1705cdef CUresult cuGreenCtxStreamCreate(CUstream* phStream, CUgreenCtx greenCtx, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil:
1706 return _driver._cuGreenCtxStreamCreate(phStream, greenCtx, flags, priority) 2)xHbV W QY3L_i
1709cdef CUresult cuLogsRegisterCallback(CUlogsCallback callbackFunc, void* userData, CUlogsCallbackHandle* callback_out) except ?CUDA_ERROR_NOT_FOUND nogil:
1710 return _driver._cuLogsRegisterCallback(callbackFunc, userData, callback_out)
1713cdef CUresult cuLogsUnregisterCallback(CUlogsCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
1714 return _driver._cuLogsUnregisterCallback(callback)
1717cdef CUresult cuLogsCurrent(CUlogIterator* iterator_out, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1718 return _driver._cuLogsCurrent(iterator_out, flags)
1721cdef CUresult cuLogsDumpToFile(CUlogIterator* iterator, const char* pathToFile, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1722 return _driver._cuLogsDumpToFile(iterator, pathToFile, flags)
1725cdef CUresult cuLogsDumpToMemory(CUlogIterator* iterator, char* buffer, size_t* size, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1726 return _driver._cuLogsDumpToMemory(iterator, buffer, size, flags)
1729cdef CUresult cuCheckpointProcessGetRestoreThreadId(int pid, int* tid) except ?CUDA_ERROR_NOT_FOUND nogil:
1730 return _driver._cuCheckpointProcessGetRestoreThreadId(pid, tid)
1733cdef CUresult cuCheckpointProcessGetState(int pid, CUprocessState* state) except ?CUDA_ERROR_NOT_FOUND nogil:
1734 return _driver._cuCheckpointProcessGetState(pid, state) 2H3
1737cdef CUresult cuCheckpointProcessLock(int pid, CUcheckpointLockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1738 return _driver._cuCheckpointProcessLock(pid, args)
1741cdef CUresult cuCheckpointProcessCheckpoint(int pid, CUcheckpointCheckpointArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1742 return _driver._cuCheckpointProcessCheckpoint(pid, args)
1745cdef CUresult cuCheckpointProcessRestore(int pid, CUcheckpointRestoreArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1746 return _driver._cuCheckpointProcessRestore(pid, args)
1749cdef CUresult cuCheckpointProcessUnlock(int pid, CUcheckpointUnlockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil:
1750 return _driver._cuCheckpointProcessUnlock(pid, args)
1753cdef CUresult cuGraphicsEGLRegisterImage(CUgraphicsResource* pCudaResource, EGLImageKHR image, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1754 return _driver._cuGraphicsEGLRegisterImage(pCudaResource, image, flags)
1757cdef CUresult cuEGLStreamConsumerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream) except ?CUDA_ERROR_NOT_FOUND nogil:
1758 return _driver._cuEGLStreamConsumerConnect(conn, stream)
1761cdef CUresult cuEGLStreamConsumerConnectWithFlags(CUeglStreamConnection* conn, EGLStreamKHR stream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1762 return _driver._cuEGLStreamConsumerConnectWithFlags(conn, stream, flags)
1765cdef CUresult cuEGLStreamConsumerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1766 return _driver._cuEGLStreamConsumerDisconnect(conn)
1769cdef CUresult cuEGLStreamConsumerAcquireFrame(CUeglStreamConnection* conn, CUgraphicsResource* pCudaResource, CUstream* pStream, unsigned int timeout) except ?CUDA_ERROR_NOT_FOUND nogil:
1770 return _driver._cuEGLStreamConsumerAcquireFrame(conn, pCudaResource, pStream, timeout)
1773cdef CUresult cuEGLStreamConsumerReleaseFrame(CUeglStreamConnection* conn, CUgraphicsResource pCudaResource, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1774 return _driver._cuEGLStreamConsumerReleaseFrame(conn, pCudaResource, pStream)
1777cdef CUresult cuEGLStreamProducerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream, EGLint width, EGLint height) except ?CUDA_ERROR_NOT_FOUND nogil:
1778 return _driver._cuEGLStreamProducerConnect(conn, stream, width, height)
1781cdef CUresult cuEGLStreamProducerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil:
1782 return _driver._cuEGLStreamProducerDisconnect(conn)
1785cdef CUresult cuEGLStreamProducerPresentFrame(CUeglStreamConnection* conn, CUeglFrame eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1786 return _driver._cuEGLStreamProducerPresentFrame(conn, eglframe, pStream)
1789cdef CUresult cuEGLStreamProducerReturnFrame(CUeglStreamConnection* conn, CUeglFrame* eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1790 return _driver._cuEGLStreamProducerReturnFrame(conn, eglframe, pStream)
1793cdef CUresult cuGraphicsResourceGetMappedEglFrame(CUeglFrame* eglFrame, CUgraphicsResource resource, unsigned int index, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil:
1794 return _driver._cuGraphicsResourceGetMappedEglFrame(eglFrame, resource, index, mipLevel)
1797cdef CUresult cuEventCreateFromEGLSync(CUevent* phEvent, EGLSyncKHR eglSync, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1798 return _driver._cuEventCreateFromEGLSync(phEvent, eglSync, flags)
1801cdef CUresult cuGraphicsGLRegisterBuffer(CUgraphicsResource* pCudaResource, GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1802 return _driver._cuGraphicsGLRegisterBuffer(pCudaResource, buffer, Flags) 2`gjp{g|gkp;Y=Y?Y@Y[Y}g~gahjg^Ybhch_Ydhal`Y{Y|Y}Y
1805cdef CUresult cuGraphicsGLRegisterImage(CUgraphicsResource* pCudaResource, GLuint image, GLenum target, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1806 return _driver._cuGraphicsGLRegisterImage(pCudaResource, image, target, Flags) 2]Y
1809cdef CUresult cuGLGetDevices(unsigned int* pCudaDeviceCount, CUdevice* pCudaDevices, unsigned int cudaDeviceCount, CUGLDeviceList deviceList) except ?CUDA_ERROR_NOT_FOUND nogil:
1810 return _driver._cuGLGetDevices_v2(pCudaDeviceCount, pCudaDevices, cudaDeviceCount, deviceList)
1813cdef CUresult cuGLCtxCreate(CUcontext* pCtx, unsigned int Flags, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil:
1814 return _driver._cuGLCtxCreate_v2(pCtx, Flags, device)
1817cdef CUresult cuGLInit() except ?CUDA_ERROR_NOT_FOUND nogil:
1818 return _driver._cuGLInit()
1821cdef CUresult cuGLRegisterBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1822 return _driver._cuGLRegisterBufferObject(buffer)
1825cdef CUresult cuGLMapBufferObject(CUdeviceptr* dptr, size_t* size, GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1826 return _driver._cuGLMapBufferObject_v2(dptr, size, buffer)
1829cdef CUresult cuGLUnmapBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1830 return _driver._cuGLUnmapBufferObject(buffer)
1833cdef CUresult cuGLUnregisterBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil:
1834 return _driver._cuGLUnregisterBufferObject(buffer)
1837cdef CUresult cuGLSetBufferObjectMapFlags(GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1838 return _driver._cuGLSetBufferObjectMapFlags(buffer, Flags)
1841cdef CUresult cuGLMapBufferObjectAsync(CUdeviceptr* dptr, size_t* size, GLuint buffer, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1842 return _driver._cuGLMapBufferObjectAsync_v2(dptr, size, buffer, hStream)
1845cdef CUresult cuGLUnmapBufferObjectAsync(GLuint buffer, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1846 return _driver._cuGLUnmapBufferObjectAsync(buffer, hStream)
1849cdef CUresult cuProfilerInitialize(const char* configFile, const char* outputFile, CUoutput_mode outputMode) except ?CUDA_ERROR_NOT_FOUND nogil:
1850 return _driver._cuProfilerInitialize(configFile, outputFile, outputMode)
1853cdef CUresult cuProfilerStart() except ?CUDA_ERROR_NOT_FOUND nogil:
1854 return _driver._cuProfilerStart() 2cZ
1857cdef CUresult cuProfilerStop() except ?CUDA_ERROR_NOT_FOUND nogil:
1858 return _driver._cuProfilerStop() 2cZ
1861cdef CUresult cuVDPAUGetDevice(CUdevice* pDevice, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1862 return _driver._cuVDPAUGetDevice(pDevice, vdpDevice, vdpGetProcAddress)
1865cdef CUresult cuVDPAUCtxCreate(CUcontext* pCtx, unsigned int flags, CUdevice device, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil:
1866 return _driver._cuVDPAUCtxCreate_v2(pCtx, flags, device, vdpDevice, vdpGetProcAddress)
1869cdef CUresult cuGraphicsVDPAURegisterVideoSurface(CUgraphicsResource* pCudaResource, VdpVideoSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1870 return _driver._cuGraphicsVDPAURegisterVideoSurface(pCudaResource, vdpSurface, flags)
1873cdef CUresult cuGraphicsVDPAURegisterOutputSurface(CUgraphicsResource* pCudaResource, VdpOutputSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1874 return _driver._cuGraphicsVDPAURegisterOutputSurface(pCudaResource, vdpSurface, flags)
1877cdef CUresult cuDeviceGetHostAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
1878 return _driver._cuDeviceGetHostAtomicCapabilities(capabilities, operations, count, dev)
1881cdef CUresult cuCtxGetDevice_v2(CUdevice* device, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1882 return _driver._cuCtxGetDevice_v2(device, ctx)
1885cdef CUresult cuCtxSynchronize_v2(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil:
1886 return _driver._cuCtxSynchronize_v2(ctx)
1889cdef CUresult cuMemcpyBatchAsync(CUdeviceptr* dsts, CUdeviceptr* srcs, size_t* sizes, size_t count, CUmemcpyAttributes* attrs, size_t* attrsIdxs, size_t numAttrs, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1890 return _driver._cuMemcpyBatchAsync_v2(dsts, srcs, sizes, count, attrs, attrsIdxs, numAttrs, hStream)
1893cdef CUresult cuMemcpy3DBatchAsync(size_t numOps, CUDA_MEMCPY3D_BATCH_OP* opList, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1894 return _driver._cuMemcpy3DBatchAsync_v2(numOps, opList, flags, hStream)
1897cdef CUresult cuMemGetDefaultMemPool(CUmemoryPool* pool_out, CUmemLocation* location, CUmemAllocationType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1898 return _driver._cuMemGetDefaultMemPool(pool_out, location, type)
1901cdef CUresult cuMemGetMemPool(CUmemoryPool* pool, CUmemLocation* location, CUmemAllocationType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1902 return _driver._cuMemGetMemPool(pool, location, type) 2_p`pbqomwjndpmxjqmyjOueqfqgqhqiqjq{k|bPu|kQu7h8h9hRuibud}kng{BZc|Bog}Bpg~BqgaCrgbCxdcCsgdCug0c.i~k
1905cdef CUresult cuMemSetMemPool(CUmemLocation* location, CUmemAllocationType type, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil:
1906 return _driver._cuMemSetMemPool(location, type, pool)
1909cdef CUresult cuMemPrefetchBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, CUmemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1910 return _driver._cuMemPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 2dg`degfg
1913cdef CUresult cuMemDiscardBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1914 return _driver._cuMemDiscardBatchAsync(dptrs, sizes, count, flags, hStream) 2dgtlul
1917cdef CUresult cuMemDiscardAndPrefetchBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, CUmemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1918 return _driver._cuMemDiscardAndPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 2`dnd
1921cdef CUresult cuDeviceGetP2PAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil:
1922 return _driver._cuDeviceGetP2PAtomicCapabilities(capabilities, operations, count, srcDevice, dstDevice)
1925cdef CUresult cuGreenCtxGetId(CUgreenCtx greenCtx, unsigned long long* greenCtxId) except ?CUDA_ERROR_NOT_FOUND nogil:
1926 return _driver._cuGreenCtxGetId(greenCtx, greenCtxId)
1929cdef CUresult cuMulticastBindMem_v2(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, CUmemGenericAllocationHandle memHandle, size_t memOffset, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1930 return _driver._cuMulticastBindMem_v2(mcHandle, dev, mcOffset, memHandle, memOffset, size, flags)
1933cdef CUresult cuMulticastBindAddr_v2(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
1934 return _driver._cuMulticastBindAddr_v2(mcHandle, dev, mcOffset, memptr, size, flags)
1937cdef CUresult cuGraphNodeGetContainingGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil:
1938 return _driver._cuGraphNodeGetContainingGraph(hNode, phGraph) 2/r
1941cdef CUresult cuGraphNodeGetLocalId(CUgraphNode hNode, unsigned int* nodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
1942 return _driver._cuGraphNodeGetLocalId(hNode, nodeId) 2{x
1945cdef CUresult cuGraphNodeGetToolsId(CUgraphNode hNode, unsigned long long* toolsNodeId) except ?CUDA_ERROR_NOT_FOUND nogil:
1946 return _driver._cuGraphNodeGetToolsId(hNode, toolsNodeId) 2|x
1949cdef CUresult cuGraphGetId(CUgraph hGraph, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1950 return _driver._cuGraphGetId(hGraph, graphId) 2!L
1953cdef CUresult cuGraphExecGetId(CUgraphExec hGraphExec, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil:
1954 return _driver._cuGraphExecGetId(hGraphExec, graphId) 2`i
1957cdef CUresult cuDevSmResourceSplit(CUdevResource* result, unsigned int nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, CU_DEV_SM_RESOURCE_GROUP_PARAMS* groupParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1958 return _driver._cuDevSmResourceSplit(result, nbGroups, input, remainder, flags, groupParams) 2aZelBjCjteV W DjEjFjGjHjIjI3J3K3L3M3N3O3
1961cdef CUresult cuStreamGetDevResource(CUstream hStream, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil:
1962 return _driver._cuStreamGetDevResource(hStream, resource, type) 27L
1965cdef CUresult cuKernelGetParamCount(CUkernel kernel, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1966 return _driver._cuKernelGetParamCount(kernel, paramCount)
1969cdef CUresult cuMemcpyWithAttributesAsync(CUdeviceptr dst, CUdeviceptr src, size_t size, CUmemcpyAttributes* attr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1970 return _driver._cuMemcpyWithAttributesAsync(dst, src, size, attr, hStream)
1973cdef CUresult cuMemcpy3DWithAttributesAsync(CUDA_MEMCPY3D_BATCH_OP* op, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1974 return _driver._cuMemcpy3DWithAttributesAsync(op, flags, hStream)
1977cdef CUresult cuStreamBeginCaptureToCig(CUstream hStream, CUstreamCigCaptureParams* streamCigCaptureParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1978 return _driver._cuStreamBeginCaptureToCig(hStream, streamCigCaptureParams)
1981cdef CUresult cuStreamEndCaptureToCig(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil:
1982 return _driver._cuStreamEndCaptureToCig(hStream)
1985cdef CUresult cuFuncGetParamCount(CUfunction func, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil:
1986 return _driver._cuFuncGetParamCount(func, paramCount)
1989cdef CUresult cuLaunchHostFunc_v2(CUstream hStream, CUhostFn fn, void* userData, unsigned int syncMode) except ?CUDA_ERROR_NOT_FOUND nogil:
1990 return _driver._cuLaunchHostFunc_v2(hStream, fn, userData, syncMode)
1993cdef CUresult cuGraphNodeGetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil:
1994 return _driver._cuGraphNodeGetParams(hNode, nodeParams) 2=i
1997cdef CUresult cuCoredumpRegisterStartCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
1998 return _driver._cuCoredumpRegisterStartCallback(callback, userData, callbackOut)
2001cdef CUresult cuCoredumpRegisterCompleteCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil:
2002 return _driver._cuCoredumpRegisterCompleteCallback(callback, userData, callbackOut)
2005cdef CUresult cuCoredumpDeregisterStartCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
2006 return _driver._cuCoredumpDeregisterStartCallback(callback)
2009cdef CUresult cuCoredumpDeregisterCompleteCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil:
2010 return _driver._cuCoredumpDeregisterCompleteCallback(callback)
2013cdef CUresult cuLogicalEndpointIdReserve(CUlogicalEndpointId* baseLeId, cuuint32_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
2014 return _driver._cuLogicalEndpointIdReserve(baseLeId, count)
2017cdef CUresult cuLogicalEndpointIdRelease(CUlogicalEndpointId baseLeId, cuuint32_t count) except ?CUDA_ERROR_NOT_FOUND nogil:
2018 return _driver._cuLogicalEndpointIdRelease(baseLeId, count)
2021cdef CUresult cuLogicalEndpointCreate(CUlogicalEndpointId leId, const CUlogicalEndpointProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
2022 return _driver._cuLogicalEndpointCreate(leId, prop)
2025cdef CUresult cuLogicalEndpointAddDevice(CUlogicalEndpointId leId, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil:
2026 return _driver._cuLogicalEndpointAddDevice(leId, dev)
2029cdef CUresult cuLogicalEndpointDestroy(CUlogicalEndpointId leId) except ?CUDA_ERROR_NOT_FOUND nogil:
2030 return _driver._cuLogicalEndpointDestroy(leId)
2033cdef CUresult cuLogicalEndpointBindAddr(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, void* ptr, cuuint64_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
2034 return _driver._cuLogicalEndpointBindAddr(leId, dev, offset, ptr, size, flags)
2037cdef CUresult cuLogicalEndpointBindMem(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, CUmemGenericAllocationHandle memHandle, cuuint64_t memOffset, cuuint64_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil:
2038 return _driver._cuLogicalEndpointBindMem(leId, dev, offset, memHandle, memOffset, size, flags)
2041cdef CUresult cuLogicalEndpointUnbind(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, cuuint64_t size) except ?CUDA_ERROR_NOT_FOUND nogil:
2042 return _driver._cuLogicalEndpointUnbind(leId, dev, offset, size)
2045cdef CUresult cuLogicalEndpointExport(void* handle, CUlogicalEndpointId leId, CUlogicalEndpointIpcHandleType handleType) except ?CUDA_ERROR_NOT_FOUND nogil:
2046 return _driver._cuLogicalEndpointExport(handle, leId, handleType)
2049cdef CUresult cuLogicalEndpointImport(CUlogicalEndpointId leId, const void* handle, CUlogicalEndpointIpcHandleType handleType) except ?CUDA_ERROR_NOT_FOUND nogil:
2050 return _driver._cuLogicalEndpointImport(leId, handle, handleType)
2053cdef CUresult cuLogicalEndpointGetLimits(cuuint64_t* bindAlignment, cuuint64_t* maxSize, const CUlogicalEndpointProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil:
2054 return _driver._cuLogicalEndpointGetLimits(bindAlignment, maxSize, prop)
2057cdef CUresult cuLogicalEndpointQuery(CUlogicalEndpointId leId, cuuint32_t count, int* queryStatus) except ?CUDA_ERROR_NOT_FOUND nogil:
2058 return _driver._cuLogicalEndpointQuery(leId, count, queryStatus)
2061cdef CUresult cuStreamBeginRecaptureToGraph(CUstream hStream, CUstreamCaptureMode mode, CUgraph hGraph, CUgraphRecaptureCallback callbackFunc, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil:
2062 return _driver._cuStreamBeginRecaptureToGraph(hStream, mode, hGraph, callbackFunc, userData)