Coverage for cuda/bindings/cydriver.pyx: 68.16%

1049 statements  

« prev     ^ index     » next       coverage.py v7.16.2, created at 2026-10-16 01:23 +0000

1# SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. 

2# 

3# SPDX-License-Identifier: Apache-2.0 

4# 

5# This code was automatically generated across versions from 12.9.0 to 13.4.1. Do not modify it directly. 

6  

7# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=99b0dd6a5b631fb108b5d2422c62f8fd4660630dda543978357a03d96c5dc201 

8from ._internal cimport driver as _driver 

9  

10cdef CUresult cuGetErrorString(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil: 

11 return _driver._cuGetErrorString(error, pStr) 2DgEgBeCeDeRb'cFgGgHgonIgSb] JgEeFe^ c lb(c)cmb*c2WVt3W4WKgLgMgWtXtnbGeNg

12  

13  

14cdef CUresult cuGetErrorName(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil: 

15 return _driver._cuGetErrorName(error, pStr) 2DgEgBeCeDeRb'cFgGgHgonIgSb] JgEeFe^ c lb(c)cmb*c2WVt3W4WKgLgMgWtXtnbGeNg

16  

17  

18cdef CUresult cuInit(unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

19 return _driver._cuInit(Flags) 2a YtZt0t1t2t3t4t5t6t7t8t9t!tg$Zk#tpn$t%t't(t)t*t+t,t-t.t/t:t;t=t?t@t[t]t^t_t`t{tqnrnsntnunvnwnxnynznAnBnCnDnEnFnGnHnInJn0kKnLnMnNnOnPnQn|t}t~taubucudueufuguhuiujukulu1kmunuoupuqu

20  

21  

22cdef CUresult cuDriverGetVersion(int* driverVersion) except ?CUDA_ERROR_NOT_FOUND nogil: 

23 return _driver._cuDriverGetVersion(driverVersion) 2a h$i$j$k$l$m$

24  

25  

26cdef CUresult cuDeviceGet(CUdevice* device, int ordinal) except ?CUDA_ERROR_NOT_FOUND nogil: 

27 return _driver._cuDeviceGet(device, ordinal) 2YtZt0t1t2t3t4t5t6t7t8t9t!t#t$t%t't(t)t*t+t,t-t.t/t:t;t=t?t@t[t]t^tVt_t`t{tqnrnsntnunvnwnxnynznAnBnCnDnEnFnGnHnInJn0kKnLnMnNnOnPnQn|t}t~tHeaubucudueufuguhuiujukulunuoupuqu

28  

29  

30cdef CUresult cuDeviceGetCount(int* count) except ?CUDA_ERROR_NOT_FOUND nogil: 

31 return _driver._cuDeviceGetCount(count) 2a 5W6W7W8W9W!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~WaXbXcXdXeXfXgXhXiXjXkXlXmXnXoXpXqXrXsXtXuXvXwXxXyXzXAXBXCXDXEXFXGXHXIXJXKXLXMXNXOXPXQXRXSXTXUXVXWXXXYXZX0X1X2X3X4XOgIePgruJeQgRg5X6X7X8X9X!X#X$X%X'X(X)X*X+X,X-X.X/X:X;X=X?X@X[X]X^X_X`X{X|X}X~XaYbYcYdYeYfYgYhYiYjYkYlYmYnYoYpYqYrYsYtYuYvYSgTg+cKeLeMeNeRnSnUgVgOeTb,c-c.c/cWgXgYgZg:cPeQeReSeTnUn0g1gTeUb;c=c?c@c2g3g4gUe5gsuVe6g7g8gWe9gXe!g#g$g%g[cYeZe0e1eVnWn'g(g2eVb]c^c_c`c)g*g+g,g{c3e4e5e6eXnYn-g.g7eWb|c}c~cad/g:g;g=gbd8e9e!e#eZn0n?g@g$eXbcdddedfd[g]g^g_ggd%e'e(e)e1n2n`g{g*eYbhdidjdkd|g}g~g+eah,ebhchdh-eeh.efhghwYhh/eih:ejhkhxYyYzYAYBYCYDYEYFYGYHYIYJYKYLYMYNYOYPYQYRYSYTYUYVYWYXYYYZY0Y1Y2Y3Y4Y5Y6Y7Y8Y9Y!Y#Y$Y%Y'Y(Y)Y*Y+Y,Y-Y.Y/Y:Y;Y=Y?Y@Y[Y]Y^Y_Y`Y{Y|Y}Y~YaZbZcZdZeZfZgZhZiZjZkZlZmZnZoZpZqZrZsZtZuZvZwZxZyZzZAZBZCZDZEZFZGZHZIZJZKZLZMZNZOZPZQZRZSZTZUZVZWZXZYZZZ0Z1Z2ZldtumduundvuwuxuyuzuAuBuCuDuEuFuGuHuIuJuKuLuMuNuOuPuQuRuSuTuUuVuWuXu3ZYu4Z5Z6Z7Z8Z9Z!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~Za0b0c0d0e0f0g0h0i0j0k0l0m0n0o0p0q0r0s0t0u0v0w0x0y0z0A0B0C0D0E0F0G0H0I0J0K0L0M0N0O0P0Q0R0S0T0U0V0W0X0Y0Z000102030405060708090!0#0$0%0'0(0)0*0+0,0-0.0/0:0;0=0?0@0[0;eodpdZu0uqd=e1u?e@erd[e2usdtd3u4u5u6uudvdwdxdydzdAdBdCdDdEdFd7u8u9u!u#u$u%u'u(u)u*u+u,u-u.u/u:u;u=u?u@u[u]u^u_u`u2k3k4k5k6k7k8k]03n9klh!k#k$k%k'k(k)k*k+k^0mh]e4nnh^e,koh_e_0ph`e5n-k.k/k:k;k=k?k@k[k`0{0|0}0~0a1n$]kqh6n^krh7n8n_ksh9n`kth!n{k|kuh#n$n}kvh%n'n~kwh(n)n{u7 alxh*n+n,n-n.n/n:n;n=n?n@n[nblclyh]ndlelzh^nflAh_nglhliljlklllmlnlolplqlrlBhChDhEhFhGhHhIhJhKhLhMh`n{n|n}n~naobocodoeofogo{eslNhhotlOhio|eulPhjo}evlQhkob1c1d1wlRhlomonooopoxlShqoylThro~ezlUhso|u}u~uavbvcvdveve1fvgvhvivjvkvlvmvnvovpvqvrvsvtvuvvvwvGdtoHduoZkvowoxoyozoAoBoCoDopnf1g1h1i1j1k1l1m1n1o1p1q1r1Eos1t1u1v1Vhw1xvFoGoHoIoJoKoLoMoNoOoPoQoRoSoToUoVoWoXoYoZo0o1o2o3o4o5o6o7o8o9o!o#o$o%o'ox1y1o$yvz1zvA1AvB1C1D1E1F1af_ bfG1(oH1I1J1K1L1M1N1O1P1Q1R1S1T1U1V1W1X1Y1Z101112131415161718191!1#1$1%1'1(1)1*1+1,1-1Bv)oCvDv*oAl+o,o-o.o/o.1:o;o=o?o@oEvFvGvHvIv/1JvKvLvMvNvOvPvQvRvSvTvUvVvWvXvYvZv0v1vp$2v3v:1[o4v;1He=1IdJdKd?1@1[1]1^1_1`1{1|1}1~1a2b2c2d2e2f2g2h2i2j2k2l2m2n2o2p2q2r25vs2t2u2v2w2x2y2z2A2B2C2D2E2F2G2H2I2J2K2L2M2N2O2P2Q2R2S2T2U2V2W2X2Y2Z20212223242526272]o8292^o_o!2#2`o{o|o}o~oapbpcpdpepfpgphpipjpkplpmpnpopppqprpsptpupvpwpxpypzpApBp$2%2CpDpEpFp'2(2)2*2+2,2GpHpIpJpKp-2.2WhLpcfdf/2:2;2BlCl=2?2DlEl@2[2]2^2_2`2{2|2}2~2a3b3c3d3e3f3g3h3i3j3k3l3m3n3o3p3q3r3s3t3u3v3w3x3y3z3A3B3C3D3E3F3G3H3I3J3K3L3M3N3O3P3Q3R3S3T3U3V3W3X3Y3Z303132333435363738393!3#3$3%3'3(3)3*3+3,3-3.3/3:3;3=3?3@3[3]3^3_3`3{3|3}3~3a4MpNp6vb4Opc4d47v8ve49v!v#v$vf4%vq$'vFlGlg4h4XhYhPpQpRpSpTpUpi4j4k4l4m4n4o4p4q4r4s4t4u4v4w4x4y4z4A4B4C4D4E4F4G4H4I4J4K4L4M4N4O4P4Q4R4S4T4U4V4W4X4Y4Z404142434445464748494!4#4$4%4'4(4)4*4+4,4-4.4/4:4;4=4?4@4(vZh0h)v1h[4]4^4_4`4{4|4}4~4a5b5c5d5e5f5g5h5i5*vj5k5l5m5n5o5p5q5r5s5t5u5v5w5x5y5z5A5B5C5D5E5F5G5H5I5J5K5L5M5N5O5P5Q5R5S5T5U5V5W5X5Y5Z505152535455565758595!5#5$5%5'5(5)5*5VpWpXp+5Yp,5Zp0p1p-52pGe.5/5:5;5=5?5@5[5]5^5_53p4p5p6p7p8p9p!p#p$p%p'p(p`5{5)p*p+p,p-p.p/p:p;p=p?p@p[p]p^p_p`p{p|p}p~paqbqcqdqeqfqgqhqiqjqkqlqmqnqoqpqqqrqsqtquqvqwqxqyqzqAqBqCqDqEqFqGqHqIqJqKqLqMqNqOqPqQqRqSqTqUq+vVq2h|5Wq}53h4hLdHl~5a6efb6XqYqff,vZq5h6h0q7hZbMd1q-vc68h9h!h2qd6e6#h$hNdIlf6g6gfh63q4qhf.v5q%h'h6q(h0bOd7q/vi6)h*h+h,hPdJlj6k6ifl68q9qjf:v!q-h.h#q/h1bQd$q;vm6:h;hb n6o6kflf=h?h%q'q@h[hRdKlp6q6mfr6(q)qnf=v*q]h^h+q_h2bSd,q-qs6.q/qt6?vu6`h{h|h}hTdLlv6w6ofx6:q;qpf@v=q~hai?qbi3bUd@q[vy6cidieifiVdMlz6A6qfB6[q]qrf]v^qgihi_qii4bWd`q^vC6jikilimiXdNlD6E6sfF6{q|qtf_v}qnioi~qpi5bYdar`vG6qirisitiZdOlH6I6ufJ6brcrvf{vdruivierwi6b0dfr|vK6xiyiziAi1dPlL6M6wfN6grhrxf}virBiCijrDi7b2dkr~vO6EiFiGiHi3dQlP6Q6yfR6lrmrzfawnrIiJiorKi8b4dprqrbwS6LiMiNiOi5dRlT6U6AfV6rrsrBfcwtrPiQiurRi9b6dvrwrdwW6SiTiX6Y6xrZ606162636465666768696!6#6$6%6'6(6)6*6+6,6-6.6/6:6;6=6?6@6[6]6^6_6`6{6|6}6~6a7b7c7d7yre7f7g7h7i7j7k7zrArBrCrNgl7m7n7o7p7q7r7s7t7u7v7w7x7y7z7DrErFrGrHrIrA7JrKrLrMrNrB7SlC7D7E7F7G71kH7I7J7K7L7M7N7O7P7Q7R7S7T7r$U7s$t$u$V7W7X7Y7Z707172737475767778797!7#7$7%7mu'7(7)7*7+7,7-7.7OrPrQrRrSrTrUrVrWrXrYrZr0r1r2r3r4rewfwgw5r6r7r8r9rhwiw!r#r$r%r'r(r)r*r+r,r-r.r/r:r;r=r?r@r/7:7;7=7?7[r]r^r@7[7]7^7_7`7{7|7}7~7a8b8c8d8e8f8g8h8i8j8k8l8m8n8o8p8q8r8s8t8u8v8w8x8y8z8A8B8C8D8E8F8G8H8I8J8K8L8M8N8O8P8Q8R8S8T8U8V8W8X8Y8Z8081828384858Tl68788898!8#8$8%8'8(8)8*8+8,8-8.8/8:8;8=8?8@8[8]8^8_8`8{8|8}8~8a9b9c9d9e9f9g9h9i9j9k9l9m9n9o9p9q9r9s9t9u9v9w9x9y9z9A9B9C9D9E9F9G9H9I9J9K9L9M9N9O9P9Q9R9S9T9U9V9W9X9Y9Z909192939495969798999!9#9$9%9'9(9)9*9+9,9-9.9/9:9;9=9?9@9

32  

33  

34cdef CUresult cuDeviceGetName(char* name, int len, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

35 return _driver._cuDeviceGetName(name, len, dev) 27dUi8 obCf!bVi#b$b%b'brcDfsctcjw8dpbWiEfqbXiYiFfGfZilhpn[9kwv$

36  

37  

38cdef CUresult cuDeviceGetUuid(CUuuid* uuid, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

39 return _driver._cuDeviceGetUuid_v2(uuid, dev) 2lh#k%k(k]kqh6n^krh7n_ksh9n`kth!n|kuh#n$n}kvh%n'n~kwh(n)nalxh*n+n,n-n.n/n:n;n=n?n@n[nclyh]nelzh^nflAh_nglhliljlklllmlnlolplqlrlBhChDhEhFhGhHhIhJhKhLhMh`n{n|n}n~naobocodoeofogoslNhhotlOhioulPhjovlQhkowlRhlomonooopoxlShqoylThrozlUhsotouoZkvowoxoyozoAoBoCoDow$f1g1h1x$y$z$A$B$C$D$E$lw0iHf1i2i3i4iIf5i6i9d7i8i9i!i!d#iUlJf_r`rSqTqUqVqF$kflf=h?hG$H$I$J$

40  

41  

42cdef CUresult cuDeviceGetLuid(char* luid, unsigned int* deviceNodeMask, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

43 return _driver._cuDeviceGetLuid(luid, deviceNodeMask, dev) 

44  

45  

46cdef CUresult cuDeviceTotalMem(size_t* bytes, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

47 return _driver._cuDeviceTotalMem_v2(bytes, dev) 

48  

49  

50cdef CUresult cuDeviceGetTexture1DLinearMaxWidth(size_t* maxWidthInElements, CUarray_format format, unsigned numChannels, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

51 return _driver._cuDeviceGetTexture1DLinearMaxWidth(maxWidthInElements, format, numChannels, dev) 

52  

53  

54cdef CUresult cuDeviceGetAttribute(int* pi, CUdevice_attribute attrib, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

55 return _driver._cuDeviceGetAttribute(pi, attrib, dev) 2a Kf2 $i#df G %i$ducN vcrbLf%dRbsbwcMf'i` ]9j k l m n o p q r s t u v w x y O z A B C D P Q R S {r|r(iFgGgVl}rWlOgIePgJeQgRg)i'd(d)dNfxc^9_9OfPfQf*iRf3 4 5 9 (b)b*byc`9~rasbs+i,i-iXlcsSgTg+cKeLeMeNeOeTb,c-c.c/cYgZg:cPeQeReSeTeUb;c=c?c@c4gUe5gVe6g7g8gWe9gXe!g#g$g%g[cYeZe0e1e2eVb]c^c_c`c+g,g{c3e4e5e6e7eWb|c}c~cad;g=gbd8e9e!e#e$eXbcdddedfd^g_ggd%e'e(e)e*eYbhdidjdkd~g+eah,ebhchdh-eeh.efhghhh/eih:ejhkhK$.imwnwdsesfsgsL$/iM${9|9}9~9a!b!+b,b-b.b/bzctb:i;i*d+dAc{ | :bubT owYlBc;b=i=bSfTf! # E Uf$ Cc% vbwbVfWfxbDc} ' U V W d ] ldtumduundvuwuxuyuzuAuBuCuDuEuFuGuH HuybIuI JuJ KuX Lu?bMuY NuZ Ou( Pu) Qu* RuSuTuUuVuWuXuYupb@b[b]bXfYfZfEcFcGcZl0l1lhsise ?ijsHcIcJc@iKc,dLcqb[iksK L c g h i lb0 zbMc]i^i_i`i(c{i+ AbBb-d.d/d^b:d;dls2l3l;eodpd~ abqd=eCb?e@erd[ebbsdtd, - . cbudvdwdxdydzdAdBdCdDdEdFdNcOc/ : ; = 7k8k9k!k$k'k)k*k+k4lmh]e4nnh^e,koh_eph`e5n-k.k/k:k;k=k?k@k[kpwc!N$O$d!]kqh6n^krh7n_k5lsh9n`k6lth!n|kuh#n$n}kvh%n'n~kwh(n)n{u7 aldbxheb*n+n,n-n.n/n:n;n=n?n@n[ncl|iyh]nel}izh^nflAh_nglhliljlklllmlnlolplqlrlBh7lCh8lDhEhFh9lGh!lHhIhJh#lKh$lLhMh`n{n|n}n~naobocodoeofogosl=dNhhotl?dOhioul@dPhjovl[dQhkowlPcRhlomono0foo1fpoxl]dShqoyl^dThrozl_dUhso|u}u~uavbvcvdvevfvgvhvivjvkvlvmv~invovpvqvrvsvtvuvvvwvtouo2fZk3fvowoxo4fyo5fzoAoBoP$CoQ$DopnajEoqwQcRcrwswtwFouwvwGowwxwywHozwAwBwCwDwEwFwGwIoJoKoHwIwJwKwLwMwNwOwPwQwRwSwTwUwVwLoWwXwMoYwZwNo0w1wOo2w3w4w5wPo6w7w8w9w!w#w$w%w'w(w)w*w+w,wQoRo-w.w/w:w;w=wSo?w@w[w]w^w_w`w{w|w}w~wToaxbxcxUodxVoWoXoYoexfxgxhxZoixjx0o1okxlxmxnxoxpxqx2o3orxsxtxux4o5o6o7ovxwxxxyxzx8oAxBxCx9oDx!o#o$o%oExFxGxHxIx'oyvzvAv_ ScbjDbAl? +o@ ,oR$S$T$`dHeEbFb{d|d}d~d_baebeKde!f!g!cedemsh!i!5vj!cjdjejfjgjhjijjjkjljmjnjU$]ofbgb^o_ohbib`o{o|o}o~oapbpcpdpepfpgphpipjpkplpmpnpopppqprpsptpupvpwpxpypzpApBpk!l!CpDpEpFpeefe6vnsos8v%l9v!v#v$v%v'v'lpsqs(lrssstsusvsojpj)lqjws0i*lHfxs1iys2izs3iAs4i+lIfBs5i,lJxrjKx-lLx.lMx/lNx:lOxsjPx;lQxCs6itj9dDs7iEs8iFs9iGs!iuj!dHs#iUl=lIs?lvjwj(v)v@l[lxjXtyjJfRxm!_r`rn!*v]l^lzjJsTcKsLsSxTxAjUxgeVxWx6f7f8fUcVc9fMs1 nbWcXc!fBj_lXxCjYx#fNsYcZcOs$fo!VpWpXp`lYpZxZp0p1p[ 2pGe0x1x2x3x4x5x6x7x8x9xPs3p4p5p6p7p8p9p!p#p$p%p'p(p`b{b!x)p#x*p$x+p%x,p'x-p(x.pQs/pRs:pSs;pTs=pUs?pVs@pWs[pXs]pYs^pZs_p0s`p1s{p2s|p3s}p4s~p5saq6sbq7scqdqeq)xfq*xgq+xhq,xiq-xjq.xkq/xlq:xmq;xnq=xoq?xpq@xqq[xrq]xsq^xtq_xuq`xvq{xwq|xxq}xyq~xzqAqBqCqDqEqFqGqHqIqJqKqLqMqNqOqPqQqRqSqTqUq+vVq2hWq3h4hLdefff0q7hZbMd1q!h2q#h$hNdgfhf6q(h0bOd7q+h,hPdifjf#q/h1bQd$qb kflf=h?h%q'q@h[hRdmfnf+q_h2bSd,q-q.q/q|h}hTdofpf?qbi3bUd@qeifiVdqfrf_qii4bWd`qlimiXdsftf~qpi5bYdarsitiZdufvferwi6b0dfrziAi1dwfxfjrDi7b2dkrGiHi3dyfzforKi8b4dprqrNiOi5dAfBfurRi9b6dvrwrp!q!xrr!s!t!u!zrArBrCrNgDrErFrGrHrIrv!JrKrLrMrNrw!x!Sly!z!A!P7OrPrQrRrSrTrUrVrWrXrYrZr0r1r2r3r4rheieje5r6r7r8r9r|b}b!r#r$r%r'r(r)r*r+r,r-r.r/r:r;r=r?r@r[r]r^rjb%f'f(f)f*f+f,f-f.f/f:f;f=f?f@fkeDjEjFjGjHjIjJjKjLjMjNjOjPjQjRjSjTjUjVjWjXjYjZj0j1j2j3j4j5j6j7j8j9j!j#j$j%j'j(j)j*j0c+j,j-j

56  

57  

58cdef CUresult cuDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, CUdevice dev, int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

59 return _driver._cuDeviceGetNvSciSyncAttributes(nvSciSyncAttrList, dev, flags) 

60  

61  

62cdef CUresult cuDeviceSetMemPool(CUdevice dev, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil: 

63 return _driver._cuDeviceSetMemPool(dev, pool) 2ay

64  

65  

66cdef CUresult cuDeviceGetMemPool(CUmemoryPool* pool, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

67 return _driver._cuDeviceGetMemPool(pool, dev) 

68  

69  

70cdef CUresult cuDeviceGetDefaultMemPool(CUmemoryPool* pool_out, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

71 return _driver._cuDeviceGetDefaultMemPool(pool_out, dev) 

72  

73  

74cdef CUresult cuDeviceGetExecAffinitySupport(int* pi, CUexecAffinityType type, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

75 return _driver._cuDeviceGetExecAffinitySupport(pi, type, dev) 

76  

77  

78cdef CUresult cuFlushGPUDirectRDMAWrites(CUflushGPUDirectRDMAWritesTarget target, CUflushGPUDirectRDMAWritesScope scope) except ?CUDA_ERROR_NOT_FOUND nogil: 

79 return _driver._cuFlushGPUDirectRDMAWrites(target, scope) 

80  

81  

82cdef CUresult cuDeviceGetProperties(CUdevprop* prop, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

83 return _driver._cuDeviceGetProperties(prop, dev) 

84  

85  

86cdef CUresult cuDeviceComputeCapability(int* major, int* minor, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

87 return _driver._cuDeviceComputeCapability(major, minor, dev) 

88  

89  

90cdef CUresult cuDevicePrimaryCtxRetain(CUcontext* pctx, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

91 return _driver._cuDevicePrimaryCtxRetain(pctx, dev) 2qnrnsntnunvnwnxnynznAnBnCnDnEnFnGnHnInJn0kKnLnMnNnOnPnQn

92  

93  

94cdef CUresult cuDevicePrimaryCtxRelease(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

95 return _driver._cuDevicePrimaryCtxRelease_v2(dev) 2V$W$X$Y$Z$0$1$2$3$4$5$6$7$8$9$!$#$$$%$'$0k($)$*$+$,$-$.$/$

96  

97  

98cdef CUresult cuDevicePrimaryCtxSetFlags(CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

99 return _driver._cuDevicePrimaryCtxSetFlags_v2(dev, flags) 

100  

101  

102cdef CUresult cuDevicePrimaryCtxGetState(CUdevice dev, unsigned int* flags, int* active) except ?CUDA_ERROR_NOT_FOUND nogil: 

103 return _driver._cuDevicePrimaryCtxGetState(dev, flags, active) 

104  

105  

106cdef CUresult cuDevicePrimaryCtxReset(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

107 return _driver._cuDevicePrimaryCtxReset_v2(dev) 

108  

109  

110cdef CUresult cuCtxCreate_v2(CUcontext* pctx, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

111 return _driver._cuCtxCreate_v2(pctx, flags, dev) 

112  

113  

114cdef CUresult cuCtxCreate_v3(CUcontext* pctx, CUexecAffinityParam* paramsArray, int numParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

115 return _driver._cuCtxCreate_v3(pctx, paramsArray, numParams, flags, dev) 

116  

117  

118cdef CUresult cuCtxCreate(CUcontext* pctx, CUctxCreateParams* ctxCreateParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

119 return _driver._cuCtxCreate_v4(pctx, ctxCreateParams, flags, dev) 2YtZt0t1t2t3t4t5t6t7t8t9t!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~taubucudueufuguhuiujukulunuoupuqu

120  

121  

122cdef CUresult cuCtxDestroy(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

123 return _driver._cuCtxDestroy_v2(ctx) 2:$;$=$?$@$[$]$^$_$`${$|$}$~$a%b%c%d%e%f%g%h%i%j%k%l%m%n%o%p%q%r%s%t%u%v%w%x%y%z%A%B%C%D%E%F%G%H%I%J%K%L%M%

124  

125  

126cdef CUresult cuCtxPushCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

127 return _driver._cuCtxPushCurrent_v2(ctx) 2Vh{lKg|lLg8s9sMgbycydyXhYh}l~l.jBjTl

128  

129  

130cdef CUresult cuCtxPopCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

131 return _driver._cuCtxPopCurrent_v2(pctx) 2eyfygyhyiyjykylymynyoypyqyrysytyuyvywyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMyNyOyPyQyRySyTyUyVyWyXyYyZy0y1y2y3y4y5y6y7y8y9y!y#y$y%y'y(y)y*y+y,y-y.y/y:y;y=y?y@y[y]y^y_y`y{y|y}y~yazbzczdzezfzgzhzizjzkzlzmznzozpzqzrzsztzuzvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z4z5z6z7z8z9z!z#z$z%z'z(z)z*z+z,z-z.z/z:z;z=z?z@z[z]z^z_z`z{z|z}z~zaAbAcAdAeAfAgAhAiAjAkAlAmAnAoApAqArAsAtAuAvAwAxAyAzAAABACADAEAFAGAHAIAJAKALAMANAOAPAQARASATAUAVAWAXAYAZA0A1A2A3A4A5A6A7A8A9A!A#A$A%A'A(A)A*A+A,A-A.A/A:A;A=A?A@A[A]A^A_A`A{A|A}A~AaBbBcBdBeBfBgBhBiBjBkBlBmBnBoBpBqBrBsBtBuBvBwBxByBzBABBBCBDBEBFBGBHBIBJBKBLBMBNBOBPBQBRBSBTBUBVBWBXBYBZB0B1B2B3B4B5B6B7B8B9B!B#B$B%B'B(B)B*B+B,B-B.B/B:B;B=B?B@B[B]B^B_B`B{B|B}B~BaCbCcCdCeCfCgChCiCjCkClCmCnCoCpCqCrCsCtCuCvCwCxCyCzCACBCCCDCECFCGCHCICJCKCLCMCNCOCPCQCRCSCTCUCVCWCXCYCZC0C1C2C3C4C5C6C7C8C9C!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}C~CaDbDcDdDeDfDgDhDiDjDkDlDmDnDoDpDqDrDsDtDuDvDwDxDyDzDADBDCDDDEDFDGDHDIDJDKDLDMDNDODPDQDRDSDTDUDVDWDXDYDZD0D1D2D3D4D5D6D7D8D9D!D#D$D%D'D(D)D*D+D,D-D.D/D:D;D=D?D@D[D]D^D_D`D{D|D}D~DaEbEcEdEeEfEgEhEiEjEkElEmEnEoEpEqErEsEtEuEvEwExEyEzEAEBECEDEEEFEGEHEam/j:jIEJE;jbmKEcmdm=jemLE?j@jMENEOEPE[j]j^j_j`j{j|j}j~jakbkckQERESETEUEVEWEXEYEZE0E1E2E3E4E5E6E7E8E9E!E#E$E%E'E(E2k3k4k5k6k)E*E+E!s#s$s%s's(s,E-E)s.E/E*s:E+s,s;E=E-s?E@E.s/s[E]E^E_E`E{E|E}E~EaFbFcFdFeFfFgFhFiFjFkFlFmFnFoFpFqFrFsFtFuFvFwFxFyFzFAFBFCFDFEFFFGFHFIFJFKFLFMFNFOFPFQFRFSFTFUFVFWFXFYFZF0F1F2F3F4F5F6F7F8F9F!F#F$F%F'F(F)F*F+F,F-F.F/F:F;F=F?F@F[F]F^F_F`F{F|F}F~FaGbGcGdGeGfGgGhGiGjGkGlGmGnGoGpGqGrGsGtGuGvGwGxGyGzGAGBGCGDGEGFGGGHGIGJGKGLGMGNGOGPGQGRGSGTGUGVGWGXGYGZG0G1G2G3G4G5G6G7G8G9G!G#G$G%G'G(G)G*G+G,G-G.G/G:G;G=G?G@GB!C![G]G^G_G`G{G|G}GD!~GaHVhE!bHcHF!G!dHeHfHgHhHiHjH{lkHKglH|lmHLgnH8soHpH9sqHMgrHsHtHuHvHwHxHyHzHAHBHCHDHEHFHGHHHIHJHKHLHMHNHOHPHQHRHSHTHUHVHWHXHYHZH0H1H2H3H4H5H6H7H8H9H!H#H$H%H'H(H)H*H+H,H-H.H/H:H;H=H?H@H[H]H^H_H`H{H|H}H~HaIbIcIdIeIfIgIhIiIjIkIlImInIoIpIqIrIsItIuIvIwIxIyIzIAIBICIDIEIFIGIHIIIJIKILIMINIOIPIQIRISITIUIVIWIXIYIZI0I1I2I3I4I5I6I7I8I9I!I#I$I%I'I(I)I*I+I,I-I.I/I:I;I=I?I@I[I]I^I_I`I{I|I}I~IaJbJcJdJeJfJgJhJiJjJkJlJmJnJoJpJqJrJsJtJuJvJwJxJyJzJAJBJCJDJEJFJGJHJIJJJKJLJMJNJOJPJQJRJSJTJUJVJWJXJYJZJ0J1J2J3J4J5J6J7J8J9J!J#J$J%J'J(J)J*J+J,J-J.J/J:J;J=J?J@J[J]J^J_J`J{J|J}J~JaKbKcKdKeKfKgKhKiKjKkKlKmKnKoKpKqKrKsKtKuKvKwKxKyKzKAKBKCKDKEKFKGKHKIKJKKKLKMKNKOKPKQKRKSKTKUKVKWKXKYKZK0K1K2K3K4K5K6K7K8K9K!K#K$K%K'K(K)K*K+K,K-K.K/Kby:K;K=K?K@K[K]K^K_K`K{K|K}K~KFlGlcyaLdybLXhYhcLdLeLfLgLhLiLjLkLlLmLnLoLpLqLrLsLtLuLvLwLxLyLzLALBLCLDLELFLGLHLILJLKLLLMLNLOLPLQLRLSLTLULVLWLXLYLZL0L1L2L3L4L5L6L7L8L9L!L#L$L%L'L(L)L*L+L,L-L.L/L:L;L=L?L@L}l[L~l]L^L_L`L{L|L}L~LaMbMcMdMeM.jfMgMhMiMjMkMlMmMnMoMpMqMrMsMtMuMvMwMxMyMzMAMBMCMDMEMFMGMHMIMJMKMLMMMBjNMOMPMQMRMSMTMUMVMWMXMYMZM0M1M2M3M4M5M6M7M8M9M!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~MaNbNcNdNeNfNgNhNiNjNkNlNmNnNoNpNqNrNsNtNuNvNwNxNyNzNANBNCNDNENFNGNHNINJNKNLNMNNNONPNQNRNSNTNUNVNWNXNYNZN0N1N2N3N4N5N6N7N8N9N!N#N$N%N'N(N)N*N+N,N-N.N/N:N;N=N?N@N[N]N^N_N`N{N|N}N~NaOfmbOcOdOeOfOgOhOiOjOkOlOmOnOoOpOqOrOsOtOuOvOwOgmxOyOzOAOhmBOCODOEOFOGOHOIOJOKOLOMONOOOPOQOROSOTOUOVOWOXOimYOZO0O1O2O3O4O5O6O7O8O9O!O#O$O%O'O(O)O*O+O,O-O.O/O:O;O=O?O@O[O]Ojm^O_O`O{O|O}O~OaPbPcPdPePfPgPhPiPjPkPlPmPnPoPpPqPrPsPtPuPkmvPwPxPyPzPAPBPCPDPEPFPGPHPIPJPKPLPMPNPOPPPQPRPlmSPTPUPVPWPXPYPZP0P1P2P3P4P5P6P7P8P9P!P#P$P%P'Pmm(P)P*P+P,P-P.P/P:P;P=P?P@P[P]P^P_P`P{P|P}P~PaQnmbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQqQrQsQtQuQvQwQxQomyQzQAQBQCQDQEQFQGQHQIQJQKQLQMQNQOQPQQQRQSQTQUQpmVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Qqm,Q-Q.Q/Q:Q;Q=Q?Q@Q[Q]Q^Q_Q`Q{Q|Q}Q~QaRbRcRdReRfRgRhRiRjRkRlRmRnRoRpRqRrRsRtRuRvRwRxRyRzRARBRCRDRERFRGRHRIRJRKRLRMRNRORPRQRRRSRTRURVRWRXRYRZR0R1R2R3R4R5R6R7R8R9R!R#R$R%R'R(R)R*R+R,R-R.R/R:R;R=R?R@R[R]R^R_R`R{R|R}R~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%TTlH!'T(T)T*T+T,T-T.T/T:T;T=T?T@T[T]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHUIUJUKULUMUNUOUPUQURUSUTUUUVUWUXUYUZU0U1U2U3U4U5U6U7U8U9U!U#U$U%U'U(U)U*U+U,U-U.U/U:U;U=U?U@U[U]U^U_U`U{U|U}U

132  

133  

134cdef CUresult cuCtxSetCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

135 return _driver._cuCtxSetCurrent(ctx) 25W6W7W8W9W!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~WaXbXcXdXeXfXgXhXiXjXkXlXmXnXoXpXqXrXsXtXuXvXwXxXyXzXAXBXCXDXEXFXGXHXIXJXKXLXMXNXOXPXQXRXSXTXUXVXWXXXYXZX0X1X2X3X4XOgIePgruJeQgRg5X6X7X8X9X!X#X$X%X'X(X)X*X+X,X-X.X/X:X;X=X?X@X[X]X^X_X`X{X|X}X~XaYbYcYdYeYfYgYhYiYjYkYlYmYnYoYpYqYrYsYtYuYvYSgTg+cKeLeMeNeRnSnUgVgOeTb,c-c.c/cWgXgYgZg:cPeQeReSeTnUn0g1gTeUb;c=c?c@c2g3g4gUe5gsuVe6g7g8gWe9gXe!g#g$g%g[cYeZe0e1eVnWn'g(g2eVb]c^c_c`c)g*g+g,g{c3e4e5e6eXnYn-g.g7eWb|c}c~cad/g:g;g=gbd8e9e!e#eZn0n?g@g$eXbcdddedfd[g]g^g_ggd%e'e(e)e1n2n`g{g*eYbhdidjdkd|g}g~g+eah,ebhchdh-eeh.efhghwYhh/eih:ejhkhxYyYzYAYBYCYDYEYFYGYHYIYJYKYLYMYNYOYPYQYRYSYTYUYVYWYXYYYZY0Y1Y2Y3Y4Y5Y6Y7Y8Y9Y!Y#Y$Y%Y'Y(Y)Y*Y+Y,Y-Y.Y/Y:Y;Y=Y?Y@Y[Y]Y^Y_Y`Y{Y|Y}Y~YaZbZcZdZeZfZgZhZiZjZkZlZmZnZoZpZqZrZsZtZuZvZwZxZyZzZAZBZCZDZEZFZGZHZIZJZKZLZMZNZOZPZQZRZSZTZUZVZWZXZYZZZ0Z1Z2ZldtumduundvuwuxuyuzuAuBuCuDuEuFuGuHuIuJuKuLuMuNuOuPuQuRuSuTuUuVuWuXu3ZYu4Z5Z6Z7Z8Z9Z!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~Za0b0c0d0e0f0g0h0i0j0k0l0m0n0o0p0q0r0s0t0u0v0w0x0y0z0A0B0C0D0E0F0G0H0I0J0K0L0M0N0O0P0Q0R0S0T0U0V0W0X0Y0Z000102030405060708090!0#0$0%0'0(0)0*0+0,0-0.0/0:0;0=0ls?02l@03l[0;eodpdZu0uqd=e1u?e@erd[e2usdtd3u4u5u6uudvdwdxdydzdAdBdCdDdEdFd7u8u9u!u#u$u%u'u(u)u*u+u,u-u.u/u:u;u=u?u@u[u]u^u_u`u2k3k4k5k6k7k8k]09k!k$k'k)k*k+k4l^0mh]e4nnh^e,koh_e_0ph`e5n-k.k/k:k;k=k?k@k[krm`0{0c!|0}0~0a1]kqh6n^krh7n_ksh9n`kth!n|kuh#n$n}kvh%n'n~kwh(n)n{ualxh*n+n,n-n.n/n:n;n=n?n@n[nblcl|iyh:s]ndlel}izh;s^nflAh_nglhliljlklllmlnlolplqlrlBhChDhEhFhGhHhIhJhKhLhMh`n{n|n}n~naobocodoeofogoslNhhotlOhioulPhjovlQhkob1c1d1[fwlPcRhN%lomonooopoxlShqoylThrozlUhso|u}u~uavbvcvdveve1fvgvhvivjvkvlvmvnvovpvqvrvsvtvuvvvwvtouoZkvowoxoyozoAoBoCoDoO%i1j1k1l1m1n1o1p1q1r1qnrnsntnunvnwnxnynznAnBnCnDnEnFnGnHnInJn0kKnLnMnNnOnPnQnQcRcP%Q%R%s1t1S%u1T%U%v1V%Vhw1W%[9~UX%x1Y%Z%0%1%2%{lyvKgz1|lzvLgA18sAvB19sC1MgD1E1F1af_ bfG1(oH1I1J1K1L1M1N1O1P1Q1R1S1T1U1V1W1X1Y1Z101112131415161718191!1#1$1%1'1(1)1*1+1,1-1Bv)oCvDv*oAl+o,oaV-o.o/o.1=s:o;obV=o?ocV@oEvFvGvHvIv/1JvKvLvMvNvOvPvQvRvSvTvUvVvWvXvYvZv0v1v2v3v:16 [o4v;1=1IdJdKd?1@1[1]1^1_1`1ce{1de|1}1~1a2b2c2d2e2f2g2h2i2j2k2l2m2n2o2p2q2r25vs2t2u2v2j!w2x2y2z2A2B2C2D2E2F2G2H2I2J2K2L2M2N2O2P2Q2R2S2T2U2V2W2X2Y2Z20212223242526272]o8292^o_o!2#2`o{o|o}o~oapbpcpdpepfpgphpipjpkplpmpnpopppqprpsptpupvpwpxpypzpApBp$2%2CpDpEpFp'2(2)2*2+2,2GpHpIpJpKp-2.2WhLpcfdf/2ee:2fe;2BlCl?s=2@s?2DlEl@2[2]2^2_2`2{2|2}2~2a3b3c3d3e3f3g3h3i3j3k3l3m3n3o3p3q3r3s3t3u3v3w3x3y3z3A3B3C3D3E3F3G3H3I3J3K3L3M3N3O3P3Q3R3S3T3U3V3W3X3Y3Z303132333435363738393!33%#3$3%3'3(3)3*3+3,3-3.3/3:3;3=3?3@3[3]3^3_3`3{3|3}3~3a4MpNp6vb4Opc4d48v%le49v!v#v$vf4%v'vFlGlg4h4XhYhPpQpRpSpTpUpi4j4k4l4m4qsn4(lo4rsp4ssq4tsr4uss4vst4oju4v4pjw4)lx4qjy4z4wsA40iB4*lC4HfD4xsE41iF4ysG42iH4zsI43iJ4AsK44iL4+lM4IfN4BsO45iP4,lQ4R4rjS4T4-lU4V4.lW4X4/lY4Z4:l0414sj2434;l4454Cs646i74tj849d94Ds!47i#4Es$48i%4Fs'49i(4Gs)4!i*4uj+4!d,4Hs-4#i.4Ul/4=l:4Is;4?l=4vj?4wj@4(vZh0h)v1h[4]4^4_4`4{4|4}4xj~4a5yjb5c5d5e5f5g5h5i5*vj5k5l5m5n5o5p5q5r5s5Jst5Tcu5Ksv5Lsw5Sxx5Txy5Ajz5UxA5geB5VxC5WxD56fE57fF58fG5UcH5VcI59fJ5MsK51 L5nbM5WcN5XcO5!fP5Q5R5I!S5J!T5K!U5V5CjW5YxX5#fY5NsZ5Yc05Zc15Os25$f35455565758595!5#5$5%5'5(5)5*5VpWpXp+5Yp,5Zp0p1p-52p.5/5:5;5=5?5@5[5]5^5_53p4p5p6p7p8p9p!p#p$p%p'p(p`5{5)p*p+p,p-p.p/p:p;p=p?p@p[p]p^p_p`p{p|p}p~paqbqcqdqeqfqgqhqiqjqkqlqmqnqoqpqqqrqsqtquqvqwqxqyqzqAqBqCqDqEqFqGqHqIqJqKqLqMqNqOqPqQqRqL!SqM!TqN!UqdV+vO!Vq2h|5Wq}53h4hLdHl~5a6efb6XqYqff,vZq5h6h0q7hZbMd1q-vc68h9h!h2qd6e6#h$hNdIlf6g6gfh63q4qhf.v5q%h'h6q(h0bOd7q/vi6)h*h+h,hPdJlj6k6ifl68q9qjf:v!q-h.h#q/h1bQd$q;vm6:h;hb n6o6kflf=h?h%q'q@h[hRdKlp6q6mfr6(q)qnf=v*q]h^h+q_h2bSd,q-qs6.q/qt6?vu6`h{h|h}hTdLlv6w6ofx6:q;qpf@v=q~hai?qbi3bUd@q[vy6cidieifiVdMlz6A6qfB6[q]qrf]v^qgihi_qii4bWd`q^vC6jikilimiXdNlD6E6sfF6{q|qtf_v}qnioi~qpi5bYdar`vG6qirisitiZdOlH6I6ufJ6brcrvf{vdruivierwi6b0dfr|vK6xiyiziAi1dPlL6M6wfN6grhrxf}virBiCijrDi7b2dkr~vO6EiFiGiHi3dQlP6Q6yfR6lrmrzfawnrIiJiorKi8b4dprqrbwS6LiMiNiOi5dRlT6U6AfV6rrsrBfcwtrPiQiurRi9b6dvrwrdwW6SiTiX6Y6Z606162636465666768696!6#6$6%6'6(6)6*6+6,6-6.6/6:6;6=6?6@6[6]6^6_6`6{6|6}6~6a7b7c7d7yre7f7g7h7i7j7k7l7m7n7o7p7q7r7s7t7u7v7w7x7y7z7A7B7SlC7D7E7F7G71kH7I7J7K7L74%M7N7O7P!Q7Q!R7R!S7T7U7S!V7W7X7Y7Z707172737475767778797!75%#7$7%7mu'7(7T!)7*7+7,7-7.7OrPrQrRrSrTrUrVrWrXrYrZr0r1r2r3r4rewfwgw5r6r7r8r9rhwiw!r#r$r%r'r(r)r*r+r,r-r.r/r:r;r=r?r@r/7:7;7=7?7[r]r^r@7[7]7^7_7`7{7|7}7~7a8b8c8d8e8f8g8h8i8j8k8l8m8n8o8p8q8r8s8t8u8v8w8x8y8z8A8B8C8D8E8F8G8H8I8J8K8L8M8N8O8P8Q8R8S8T8U8V8W8X8Y8Z8081828384858Tl68788898!8#8$8%8'8(8)8*8+8,8-8.8/8:8;8=8?8@8[8]8^8_8`8{8|8}8~8a9b9c9d9e9f9g9h9i9j9k9l9m9n9o9p9q9r9s9t9u9v9w9x9y9z9A9B9C9D9E9F9G9H9I9J9K9L9M9N9O9P9Q9R9S9T9U9V9W9X9Y9Z909192939495969798999!9#9$9%9'9(9)9*9+9,9-9.9/9:9;9=9?9@9

136  

137  

138cdef CUresult cuCtxGetCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

139 return _driver._cuCtxGetCurrent(pctx) 2a eyfygyhyiyjykylymynyoypyqyrysytyuyvywyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMyNyOyPyQyRySyTyUyVyWyXyYyZy0y1y2y3y4y5y6y7y8y9y!y#y$y%y'y(y)y*y+y,y-y.y/y:y;y=y?y@y[y]y^y_y`y{y|y}y~ysmazbzczdzezfzgzhzizjzkzlzmznzozpzqzrzsztzuzvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzLzMzNzOzPz3 Qz4 Rz5 Sz9 Tz(bUz)bVz*bWzycXzYzZz0z1z2z3z4z5z6z7z8z9z!z#z$z%z'z(z)z*z+z,z-z.zUg/zVg:z;zTb=z,c?z-c@z.c[z/c]zWg^zXg_z`z{z|z}z~zaAbAcAdA0geA1gfAgAUbhA;ciA=cjA?ckA@clA2gmA3gnAoApAqArAsAtAuAvAwAxAyAzAAABACADAEAFAGAHAIAJA'gKA(gLAMAVbNA]cOA^cPA_cQA`cRA)gSA*gTAUAVAWAXAYAZA0A1A2A-g3A.g4A5AWb6A|c7A}c8A~c9Aad!A/g#A:g$A%A'A(A)A*A+A,A-A.A?g/A@g:A;AXb=Acd?Add@Aed[Afd]A[g^A]g_A`A{A|A}A~AaBbBcBdB`geB{gfBgBYbhBhdiBidjBjdkBkdlB|gmB}gnBoBpBqBrBsBtBuBvBwBxByBzBABBBCBDBEBFBGBHgHBIBJBKBLBeVMBNBOBPBQBRBSBTBUBVBWBXBYBIgZB0B1B2B3B4B5B6B7B+b8B9Btm!Bum#Bvm$Bwm%B,b'B-b(B.b)B/b*B+B,B-B.B/B:B;Btb=B?B@B[B1c]B2c^B3c_B4c`B#b{B$b|B%b}B'b~BaCbCcCdCeCfCgChCiCjCkClC{ mCkbnC| oC:bpCqCrCsCtCuCvCwC=bxCyCzC! AC# BCE CCDC$ ECCcFC% GCvbHCwbICJCKCxbLCMCNCOCPCQCRC]fSCTCUCVCWCXCYCZC0C1C2C3C4Cd 5C6C7C~b8C9C!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}C~CaDbDcDdDeDfDgDhDiDjDkDlDmDnDoDpDqDrDsDtDGbuDHbvDIbwDacxDbcyDzDADBDCDDDEDFDGDccHDdcIDecJD5cKD6cLDMDNDODPDQDRDSDTDfcUDgcVDhcWD7cXD8cYDZD0D1D2D3D4De 5D6D9c7Dle8D9D!D#D$D%D'D(D)D*DJb+DKb,DLb-D!c.D#c/D:D;D=D?D@D[D]D^D_D`DMb{DNb|DOb}Dic~DjcaEbEcEdEeEK fEL gEF hEc iEjEkElEkcmElcnEmeoEpEqErEsEtEuEvEwExEyEzEAEBECEDEEEFEGEHEam/j:jIEJE;jbmKEcmdm=jemLE?j@jMENEOEPE[j]j^j_j`j{j|j}j~jakbkckQERESETEUEVEWEXEYEZE0E1E2E3E4E5E6E7E8E9E!E#E$E%E'E(E2k3k4k5k6k)E*E+E!s#s$s%s's(s,E-E)s.E/E*s:E+s,s;E=E-s?E@E.s/s[E]E^E_E`E{E|E}E~EaFbFcFdFeFfFgFhFiFjFkFlFmFnFoFpFqFrFsFtFuFvFwFxFyFzFAFBFCFDFEFFFGFHFIFJFKFLFMFNFOFPFQFRFSFTFUFVFWFXFYFZF0F1F2F3F4F5F6F7F8F9F!F#F$F%F'F(F)F*F+F,F-F.F/F:F;F=F?F@F[F]F^F_F`F{F|F}F~FaGbGcGdGeGfGgGhGiGjGkGlGmGnGoGpGqGrGsGtGuGvGwGxGyGzGAGBGCGDGEGFGGGHGIGJGKGLGMGNGOGPGQGRGSGTGUGVGWGXGYGZG0G1G2G3G4G5G6G7G8G9G!G#G$G%G'G(G)G*G+G,G-G.G/G:G;G=G?G@GEoqwQcB!RcC![G]G^G_G`G{G|G}GD!~GaHVhE!bHxvrwswtwFouwvwGowwxwywHozwAwBwCwDwEwFwGwIoJoKoHwIwJwKwLwMwNwOwPwQwRwSwTwUwVwLoWwXwMoYwZwNo0w1wOo2w3w4w5wPo6w7w8w9w!w#w$w%w'w(w)w*w+w,wQoRo-w.w/w:w;w=wSo?w@w[w]w^w_w`w{w|w}w~wToaxbxcxUodxVoWoXoYoexfxgxhxZoixjx0o1okxlxmxnxoxpxqx2o3orxsxtxux4o5o6o7ovxwxxxyxzx8oAxBxCx9oDx!o#o$o%oExFxGxHxIx'ocHF!~UG!dHeHfHy16%kwU!gHhHiHjHlw{lkHKglH|lmHLgnHoHpH9sqHMgrHsHtHaf_ bfuH(ovHwHxHyHzHAHBHCHDHEHFHGHHHIHJHKHLHMHNHOHPHQHRHSHTHUHVHWHXHYHZH0H1H2H3H4H5H6H7H8HfV9H!H#H$H%H'H? (H@ )HaV*H+H,H-H=s.H/HbV:H;HcV=H?H@H[H]H^H_H`H{H|H}H~HaIbIcIdIeIfIgIhIiIjIkIlImInIoIV!pIqI6 rIW!sItIHeuIIdJdKdvIwIxIyIzIAIBICIDIEIFIGIHIIIJIKILIMINIOIPIQIRISITIUIVIWIXIYIZI0I1I2I3I4I5I6I7I8I9I!I#I$I%I'I(I)I*I+I,I-I.I/I:I;I=I?I@I[I]I^I_I`I{I|I}I~IaJbJcJdJeJfJgJhJiJjJkJlJmJnJoJpJqJrJsJtJuJvJwJxJyJzJAJBJCJDJEJFJGJHJIJJJKJLJMJNJOJPJQJRJSJTJUJVJWJXJYJZJ0J1J2J3J4JGpHpIpJpKp5J6JWhLpcfdf7J8J9J!J#J$J%J'J(J)J*J+J,J-J.J/J:J;J=J?J@J[J]J^J_J`J{J|J}J~JaKbKcKdKeKfKgKhKiKjKkKlKmKnKoKpKqKrKsKtKuKvKwKxKyKzKAKBKCKDKEKFKGKHKIKJKKKLKMKNKOKPKQKRKSKTKUKVKWKXKYKZK0K1K2K3K4K5K6K7K8K9K!K#K$K%K'K(K)K*K+K,K-K.K/Kby:KMpNp;K=KOp?K@K[K]K^K_K`K{K|K}K~KFlGlcyaLdybLXhYhPpQpRpSpTpUpcLdLeLfLgLhLiLjLkLlLmLnLoLpLqLrLsLtLuLvLwLxLyLzLALBLCLDLELFLGLHLILJLKLLLMLNLOLPLQLRLSLTLULVLWLXLYLZL0L1L2L3L4L5L6L7L8L9L!L#L$L%L'L(L)L*L+L,L-L.L/LZh0h:L1h;L=L?L@L}l[L~l]L^L_L`L{L|L}L~LaMbMcMdMeM.jfMgMhMiMjMkMlMmMnMoMpMqMrMsMtMuMvMwMxMyMzMAMBMCMDMEMFMGMHMIMJMKMLMMMBjNMOMPMQMRMSMTMUMVMWMXMYMZM0M1M2M3M4M5M6M7M8M9M!M#M$M%M'M(M)M*M+M,M-M.M/M:M;M=MGe?M@M[M]M^M_M`M{M|M}M~MaNbNcNdNeNfNgNhNiNjNkNlNmNnNoNpNqNrNsNtNuNvNwNxNyNzNANBNCNDNENFNGNHNINJNKNLNMNNNONPNQNRNSNTNUNVNWNXNYNZN0N1N2N3N4N5N6N7N8N9N!N#N$N%N'N(N)N*N+N,N-N.N/N:N;N=N?N@N[N]N^N_N`N{N|N}N~NaOfmbOHlcOdOeOfOgOhOiOjOkOlO5hmO6hnOoOpOZbqOMdrOsOtOuO8hvO9hwOgmxOyOzOAOhmBOIlCODOEOFOGOHOIOJOKOLO%hMO'hNOOOPO0bQOOdROSOTOUO)hVO*hWOXOimYOJlZO0O1O2O3O4O5O6O7O8O-h9O.h!O#O$O1b%OQd'O(O)O*O:h+O;h,Ob -O.O/O:O;O=O?O@O[O]Ojm^OKl_O`O{O|O}O~OaPbPcPdP]heP^hfPgPhP2biPSdjPkPlPmPnPoPpPqPrP`hsP{htPuPkmvPLlwPxPyPzPAPBPCPDPEPFP~hGPaiHPIPJP3bKPUdLPMPNPOPciPPdiQPRPlmSPMlTPUPVPWPXPYPZP0P1P2Pgi3Phi4P5P6P4b7PWd8P9P!P#Pji$Pki%P'Pmm(PNl)P*P+P,P-P.P/P:P;P=Pni?Poi@P[P]P5b^PYd_P`P{P|Pqi}Pri~PaQnmbQOlcQdQeQfQgQhQiQjQkQlQuimQvinQoQpQ6bqQ0drQsQtQuQxivQyiwQxQomyQPlzQAQBQCQDQEQFQGQHQIQBiJQCiKQLQMQ7bNQ2dOQPQQQRQEiSQFiTQUQpmVQQlWQXQYQZQ0Q1Q2Q3Q4Q5QIi6QJi7Q8Q9Q8b!Q4d#Q$Q%Q'Q(QLi)QMi*Q+Qqm,QRl-Q.Q/Q:Q;Q=Q?Q@Q[Q]QPi^QQi_Q`Q{Q9b|Q6d}Q~QaRbRcRSidRTieRX!fRgRxrhRiRjRkRlRmRnRoRpRqRrRsRtRuRvRwRxRyRzRARBRCRDRERFRGRHRIRJRKRLRMRNRORPRQRRRSRTRURVRWRyrXRYRZR0R1R2R3RzrArBrCrNg4R5R6R7R8R9R!R#R$R%R'R(R)R*R+RDrErFrGrHrIr,RJrKrLrMrNr-RSl.R/R:R;R=R?R1k@R[R]R^R_R`R{R|R}R~RaSbScSdSeSfSgShSiSjSkSlSmSnSoSpSqSrSsStSuSvSwSxSySzSASBSCSDSESFSGSHSISJSKSLSMSNSOSPSQSRSSSTSUSVSWSXSYSheZSie0Sje1S2S3S4S5S6S|b7S}b8S9S!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%TTlH!'T(T)T*T+T,T-T.T/T:T;T=T?T@T[T]T^T_T`T{T|T}T~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHUIUJUKULUMUNUOUPUQURUSUTUUUVUWUXUYUZU0U1U2U3U4U5U6U7U8U9U!U#U$U%U'U(U)U*U+U,U-U.U/U:U;U=U?U@U[U]U^U_U`U{U|U}U

140  

141  

142cdef CUresult cuCtxGetDevice(CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil: 

143 return _driver._cuCtxGetDevice(device) 2a 7%Y!7dDggVEgZ!xm[sdkBeCeDe8%]sKf^s^f_f`f{f_s2 $i#df neG %i9%`s$ducN vc{srbLfhV|s%dRb'csb!%wcMf'iym#%` ]9j k l m n o p q r s t u v w x y O z A B C D P Q R S {r|r(iFg0!GgVl}rWlOgIePgJeQgRg)iekfkgkhkik'd(d)dNfxc|fjkkkOfPfQf*iRf3 4 5 9 (b)b*byc~rasbs+i,i-iXlcsSgTg+cKeLeMeNeOeTb,c-c.c/cYgZg:cPeQeReSeTeUb;c=c?c@c4gUe5gVe6g7g8gWe9gXe!g#g$g%g[cYeZe0e1e2eVb]c^c_c`c+g,g{c3e4e5e6e7eWb|c}c~cad;g=gbd8e9e!e#e$eXbcdddedfd^g_ggd%e'e(e)e*eYbhdidjdkd~g+eah,ebhchdh-eeh.efhghhh/eih:ejhkh.imwnwdsesfsgs/i{9|9}9~9a!b!+bUi,b-b.b/b8 obCflkmkzctb}s:iiVmcnk;ijV*d+d}f~fAc{ kb| :bubT owYlBc;b=i=bSfTf! # E Uf$ Cc% vbwbVfWfxbDcDfok} ' U V W d ] H ybI J X ?bY Z ( ) * $%pbPbagbgzmAm@b[b]bGbHbIbacbcBm~satkVlVXfYfZfccdcec5c6ccgoepeCmDmEcFcGcfcgchc7c8cZl0l1lhsis?ijsQbqerepkqkHcIcJcJbKbLb!c#c@i^ dgegEmFmKc,dLcMbNbObicjcqb[ikslbFfGf0 zbMcZi]i^i_i`i(c{i+ ls2l3l;eodpdZu0uqd=e1u?e@erd[e2usdtd, 3u- 4u. 5u6uudvdwdxdydzdAdBdCdDdEdFd7u8u9u!u#u$u%u'u(u: )u; *u+u= ,u-u.u/u:u;u=u?u@u[u]u^u_u`u7k8k%%9k!k$k'k)k*k+k4lmh]ese4nnh^e,koh_e1!ph2!`e5n-k.k/k:k;k=k?k@k[krmqhrhshthuhvhwhxhyhzhAhBhChDhEhFhGhHhIhJhKhLhMhNhOhPhQhRhShThUh'%(%)%*%+%,%EoqwQcRc-%.%xvrwswtwFouwvwGowwxwywHozwAwBwCwDwEwFwGwIoJoKoHwIwJwKwLwMwNwOwPwQwRwSwTwUwVwLoWwXwMoYwZwNo0w1wOo2w3w4w5wPo6w7w8w9w!w#w$w%w'w(w)w*w+w,wQoRo-w.w/w:w;w=wSo?w@w[w]w^w_w`w{w|w}w~wToaxbxcxUodxVoWoXoYoexfxgxhxZoixjx0o1okxlxmxnxoxpxqx2o3orxsxtxux4o5o6o7ovxwxxxyxzx8oAxBxCx9oDx!o#o$o%oExFxGxHxIx'o~UkwU!lw/%af_ bf:%(o;%3!4!5!6!7!8!Sc9!!!#!$!%!mVbtbjctdt'!etftgthtGm(!)!*!+!itjt,!-!.!/!:!;!ktHm=!?!aV=sbVcV6 IdJdKde!f!g!cedemsh!i!]ofbgb^o_ohbib=%`o{o|o?%}o~oapbpcpdpepfpgphpipjpkplpmpnpopppqprpsptpupvpwpxpypzpApBpk!l!CpDpEpFpGpHpIpJpKpWhLpcfdfMpNpOp%lFlGlXhYhPpQpRpSpTpUp@%qs(lrssstsusvsojpj)lqjws0i*lHfxs1iys2izs3iAs4i+lIfBs5i,lJxrjKx-lLx.lMx/lNx:lOxsjPx;lQxCs6itj9dDs7iEs8iFs9iGs!iuj!dHs#iUl=lIs?lvjwjZh0h1hxjyjJfm!_r`rn!nVoV]l^lzjJsTcKsLsSxTxAjUxgeVxWx6f7f8fUcVc9fMs1 nbWcXc!fBj_lI!J!K!XxCjYx#fNsYcZcOs$fo!Vp@!WpXp`lYpZxZp[!0p]!1p[ 2pGe0x1x2x3x4x5x6x7x8x9xPs3p4p5p6p7p8p9p!p#p$p%p'p(p!x)p#x*p$x+p%x,p'x-p(x.pQs/pRs:pSs;pTs=pUs?pVs@pWs[pXs]pYs^pZs_p0s`p1s{p2s|p3s}p4s~p5saq6sbq7scq[%dq]%eq)xfq*xgq+xhq,xiq-xjq.xkq/xlq:xmq;xnq=xoq?xpq@xqq[xrq]xsq^xtq_xuq`xvq{xwq|xxq}xyq~xzq^%Aq^!Bq_!Cq`!Dq{!Eq|!Fq}!Gq~!Hqa#Iqb#Jqc#Kqd#Lqe#Mqf#Nqg#Oqh#Pqi#QqRqWq3hLdefff0q7hZbMd1q2q#hNdgfhf6q(h0bOd7q+hPdifjf#q/h1bQd$qb %q'q@hRdmfnf+q_h2bSd,q-q.q/q|hTdofpf?qbi3bUd@qeiVdqfrf_qii4bWd`qliXdsftf~qpi5bYdarsiZdufvferwi6b0dfrzi1dwfxfjrDi7b2dkrGi3dyfzforKi8b4dprqrNi5dAfBfurRi9b6dvrwrX!p!q!xrr!s!t!u!yrzrArBrCrNgDrErFrGrHrIrv!JrKrLrMrNrw!x!Sly!z!1k_%A!P!Q!R!`%{%S!|%}%~%a'b'c'd'e'pVf'g'h'i'j'k'l'm'n'o'p'j#q'T!k#r'lts'OrPrQrRrSrTrUrVrWrXrYrZr0r1r2r3r4rheewiefwjegw5r6r7r8r9r|bhw}biw!r#r$r%r'r(r)r*r+r,r-r.r/r:r;r=r?r@r[r]r^rt'u'v'w'x'y'z'A'B'C'D'E'jbF'G'%fH'qVI'J'K'L'M'N'O'rVP'Q'l#R'm#mtS'T'U'V''f(f)f*f+f,fW'-f.f/f:f;fX'Y'=fZ'0'1'2'?f3'@f4'5'6'7'8'9'!'#'$'%'

144  

145  

146cdef CUresult cuCtxGetFlags(unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

147 return _driver._cuCtxGetFlags(flags) 

148  

149  

150cdef CUresult cuCtxSetFlags(unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

151 return _driver._cuCtxSetFlags(flags) 

152  

153  

154cdef CUresult cuCtxGetId(CUcontext ctx, unsigned long long* ctxId) except ?CUDA_ERROR_NOT_FOUND nogil: 

155 return _driver._cuCtxGetId(ctx, ctxId) 

156  

157  

158cdef CUresult cuCtxSynchronize() except ?CUDA_ERROR_NOT_FOUND nogil: 

159 return _driver._cuCtxSynchronize() 2eyfygyhyiyjykylymynyoypyqyrysytyuyvywyxyyyzyAyByCyDyEyFyGyHyIyJyKyLyMyNyOyPyQyRySyTyUyVyWyXyYyZy0y1y2y3y4y5y6y7y8y9y!y#y$y%y'y(y)y*y+y,y-y.y/y:y;y=y?y@y[y]y^y_y`y{y|y}y~yazbzczdzezfzgzhzizjzkzlzmznzozpzqzrzsztzuzvzwzxzyzzzAzBzCzDzEzFzGzHzIzJzKzLzMzNzOzPzQzRzSzTzUzVzWzXzYzZz0z1z2z3z4z5z6z7z8z9z!z#z$z%z'z(z)z*z+z,z-z.z/z:z;z=z?z@z[z]z^z_z`z{z|z}z~zaAbAcAdAeAfAgAhAiAjAkAlAmAnAoApAqArAsAtAuAvAwAxAyAzAAABACADAEAFAGAHAIAJAKALAMANAOAPAQARASATAUAVAWAXAYAZA0A1A2A3A4A5A6A7A8A9A!A#A$A%A'A(A)A*A+A,A-A.A/A:A;A=A?A@A[A]A^A_A`A{A|A}A~AaBbBcBdBeBfBgBhBiBjBkBlBmBnBoBpBqBrBsBtBuBvBwBxByBzBABBBCBDBEBFBGBHBIBJBKBLBMBNBOBPBQBRBSBTBUBVBWBXBYBZB0B1B2B3B4B5B6B7B8B9B!B#B$B%B'B(B)B*B+B,B-B.B/B:B;B=B?B@B[B]B^B_B`B{B|B}B~BaCbCcCdCeCfCgChCiCjCkClCmCnCoCpCqCrCsCtCuCvCwCxCyCzCACBCCCDCECFCGCHCICJCKCLCMCNCOCPCQCRCSCTCUCVCWCXCYCZC0C1C2C3C4C5C6C7C8C9C!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}C~CaDbDcDdDeDfDgDhDiDjDkDlDmDnDoDpDqDrDsDtDuDvDwDxDyDzDADBDCDDDEDFDGDHDIDJDKDLDMDNDODPDQDRDSDTDUDVDWDXDYDZD0D1D2D3D4D5D6D7D8D9D!D#D$D%D'D(D)D*D+D,D-D.D/D:D;D=D?D@D[D]D^D_D`D{D|D}D~DaEbEcEdEeEfEgEhEiEjEkElEmEnEoEpEqErEsEtEuEvEwExEyEzEAEBECEDEEEFEGEHEam/j:jIEJE;jbmKEcmdm=jemLE?j@jMENEOEPE[j]j^j_j`j{j|j}j~jakbkckQERESETEUEVEWEXEYEZE0E1E2E3E4E5E6E7E8E9E!E#E$E%E'E(E2k3k4k5k6k)E*E+E!s#s$s%s's(s,E-E)s.E/E*s:E+s,s;E=E-s?E@E.s/s[E]E^E_E`E{E|E}E~EaFbFcFdFeFfFgFhFiFjFkFlFmFnFoFpFqFrFsFtFuFvFwFxFyFzFAFBFCFDFEFFFGFHFIFJFKFLFMFNFOFPFQFRFSFTFUFVFWFXFYFZF0F1F2F3F4F5F6F7F8F9F!F#F$F%F'F(F)F*F+F,F-F.F/F:F;F=F?F@F[F]F^F_F`F{F|F}F~FaGbGcGdGeGfGgGhGiGjGkGlGmGnGoGpGqGrGsGtGuGvGwGxGyGzGAGBGCGDGntEG)cFGmbGGHGIGotJGKG*cLGMGfgNGOGImPGrkQGteRGSGTGUGVGueWGXGYGZG0G1G2G3G4G5G6G7G8G9G!G#G$G%G'G(G)G*G+G,G-G.G/G:G;G=G?G@G[G]G^G_G`G{G|G}G~GaHbHcHdHeHfHgHhHiHjHkHlHmHnHoHpHqHrHsHtHuHvHwHxHyHzHAHBHCHDHEHFHGHHHIHJHKHLHMHNHOHPHQHRHSHTHUHVHWHXHYHZH0H1H2H3H4H5H6H7H8H9H!H#H$H%H'H(H)H*H+H,H-H.H/H:H;H=H?H@H[H]H^H_H`H{H|H}H~HaIbIcIdIeIfIgIhIiIjIkIlImInIoIpIqIrIsItIuIvIwIxIyIzIAIBICIDIEIFIGIHIIIJIKILIMINIOIPIQIRISITIUIVIWIXIYIZI0I1I2I3I4I5I6I7I8I9I!I#I$I%I'I(I)I*I+I,I-I.I/I:I;I=I?I@I[I]I^I_I`I{I|I}I~IaJbJcJdJeJfJgJhJiJjJkJlJmJnJoJpJqJrJsJtJuJvJwJxJyJzJAJBJCJDJEJFJGJHJIJJJKJLJMJNJOJPJQJRJSJTJUJVJWJXJYJZJ0J1J2J3J4J5J6J7J8J9J!J#J$J%J'J(J)J*J+J,J-J.J/J:J;J=J?J@J[J]J^J_J`J{J|J}J~JaKbKcKdKeKfKgKhKiKjKkKlKmKnKoKpKqKrKsKtKuKvKwKxKyKzKAKBKCKDKEKFKGKHKIKJKKKLKMKNKOKPKQKRKSKTKUKVKWKXKYKZK0K1K2K3K4K5K6K7K8K9K!K#K$K%K'K(K)K*K+K,K-K.K/K:K;K=K?K@K[K]K^K_K`K{K|K}K~KaLbLcLdLeLfLgLhLiLjLkLlLmLnLoLpLqLrLsLtLuLvLwLxLyLzLALBLCLDLELFLGLHLILJLKLLLMLNLOLPLQLRLSLTLULVLWLXLYLZL0L1L2L3L4L5L6L7L8L9L!L#L$L%L'L(L)L*L+L,L-L.L/L:L;L=L?L@L[L]L^L_L`L{L|L}L~LaMbMcMdMeMfMgMhMiMjMkMlMmMnMoMpMqMrMsMtMuMvMAjwMxMgeyMzMAMBMCMDMEMFMGMHM1 IMnbJMWcKMXcLM!fMMNMOMPMQMRMSMTMUMVMWMXMYMZM$f0M1M2M3M4M5M6M7M8M9M!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~MaNbNcNdNeNfNgNhNiNjNkNlNmNnNoNpNqNrNsNtNuNvNwNxNyNzNANBNCNDNENFNGNHNINJNKNLNMNNNONPNQNRNSNTNUNVNWNXNYNZN0N1N2N3N4N5N6N7N8N9N!N#N$N%N'N(N)N*N+N,N-N.N/N:N;N=N?N@N[N]N^N_N`N{N|N}N~NaOfmbOcOdOeOfOgOhOiOjOkOlOmOnOoOpOqOrOsOtOuOvOwOgmxOyOzOAOhmBOCODOEOFOGOHOIOJOKOLOMONOOOPOQOROSOTOUOVOWOXOimYOZO0O1O2O3O4O5O6O7O8O9O!O#O$O%O'O(O)O*O+O,O-O.O/O:O;O=O?O@O[O]Ojm^O_O`O{O|O}O~OaPbPcPdPePfPgPhPiPjPkPlPmPnPoPpPqPrPsPtPuPkmvPwPxPyPzPAPBPCPDPEPFPGPHPIPJPKPLPMPNPOPPPQPRPlmSPTPUPVPWPXPYPZP0P1P2P3P4P5P6P7P8P9P!P#P$P%P'Pmm(P)P*P+P,P-P.P/P:P;P=P?P@P[P]P^P_P`P{P|P}P~PaQnmbQcQdQeQfQgQhQiQjQkQlQmQnQoQpQqQrQsQtQuQvQwQxQomyQzQAQBQCQDQEQFQGQHQIQJQKQLQMQNQOQPQQQRQSQTQUQpmVQWQXQYQZQ0Q1Q2Q3Q4Q5Q6Q7Q8Q9Q!Q#Q$Q%Q'Q(Q)Q*Q+Qqm,Q-Q.Q/Q:Q;Q=Q?Q@Q[Q]Q^Q_Q`Q{Q|Q}Q~QaRbRcRdReRfRgRhRiRjRkRlRmRnRoRpRqRrRsRtRuRvRwRxRyRzRARBRCRDRERFRGRHRIRJRKRLRMRNRORPRQRRRSRTRURVRWRXRYRZR0R1R2R3R4R5R6R7R8R9R!R#R$R%R'R(R)R*R+R,R-R.R/R:R;R=R?R@R[R]R^R_R`R{R|R}R~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~TaUbUcUdUeUfUgUhUiUjUkUlUmUnUoUpUqUrUsUtUuUvUwUxUyUzUAUBUCUDUEUFUGUHUIUJUKULUMUNUOUPUQURUSUTUUUVUWUXUYUZU0U1U2U3U4U5U6U7U8U9U!U#U$U%U'U(U)U*U+U,U-U.U/U:U;U=U?U@U[U]U^U_U`U{U|U}U

160  

161  

162cdef CUresult cuCtxSetLimit(CUlimit limit, size_t value) except ?CUDA_ERROR_NOT_FOUND nogil: 

163 return _driver._cuCtxSetLimit(limit, value) 

164  

165  

166cdef CUresult cuCtxGetLimit(size_t* pvalue, CUlimit limit) except ?CUDA_ERROR_NOT_FOUND nogil: 

167 return _driver._cuCtxGetLimit(pvalue, limit) 

168  

169  

170cdef CUresult cuCtxGetCacheConfig(CUfunc_cache* pconfig) except ?CUDA_ERROR_NOT_FOUND nogil: 

171 return _driver._cuCtxGetCacheConfig(pconfig) 

172  

173  

174cdef CUresult cuCtxSetCacheConfig(CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil: 

175 return _driver._cuCtxSetCacheConfig(config) 

176  

177  

178cdef CUresult cuCtxGetApiVersion(CUcontext ctx, unsigned int* version) except ?CUDA_ERROR_NOT_FOUND nogil: 

179 return _driver._cuCtxGetApiVersion(ctx, version) 

180  

181  

182cdef CUresult cuCtxGetStreamPriorityRange(int* leastPriority, int* greatestPriority) except ?CUDA_ERROR_NOT_FOUND nogil: 

183 return _driver._cuCtxGetStreamPriorityRange(leastPriority, greatestPriority) 2''('

184  

185  

186cdef CUresult cuCtxResetPersistingL2Cache() except ?CUDA_ERROR_NOT_FOUND nogil: 

187 return _driver._cuCtxResetPersistingL2Cache() 

188  

189  

190cdef CUresult cuCtxGetExecAffinity(CUexecAffinityParam* pExecAffinity, CUexecAffinityType type) except ?CUDA_ERROR_NOT_FOUND nogil: 

191 return _driver._cuCtxGetExecAffinity(pExecAffinity, type) 

192  

193  

194cdef CUresult cuCtxRecordEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

195 return _driver._cuCtxRecordEvent(hCtx, hEvent) 

196  

197  

198cdef CUresult cuCtxWaitEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

199 return _driver._cuCtxWaitEvent(hCtx, hEvent) 

200  

201  

202cdef CUresult cuCtxAttach(CUcontext* pctx, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

203 return _driver._cuCtxAttach(pctx, flags) 

204  

205  

206cdef CUresult cuCtxDetach(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

207 return _driver._cuCtxDetach(ctx) 

208  

209  

210cdef CUresult cuCtxGetSharedMemConfig(CUsharedconfig* pConfig) except ?CUDA_ERROR_NOT_FOUND nogil: 

211 return _driver._cuCtxGetSharedMemConfig(pConfig) 

212  

213  

214cdef CUresult cuCtxSetSharedMemConfig(CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil: 

215 return _driver._cuCtxSetSharedMemConfig(config) 

216  

217  

218cdef CUresult cuModuleLoad(CUmodule* module, const char* fname) except ?CUDA_ERROR_NOT_FOUND nogil: 

219 return _driver._cuModuleLoad(module, fname) 

220  

221  

222cdef CUresult cuModuleLoadData(CUmodule* module, const void* image) except ?CUDA_ERROR_NOT_FOUND nogil: 

223 return _driver._cuModuleLoadData(module, image) 2AbBb-d.d/d^b:d;dEbFb{d|d}d~d_baebe

224  

225  

226cdef CUresult cuModuleLoadDataEx(CUmodule* module, const void* image, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil: 

227 return _driver._cuModuleLoadDataEx(module, image, numOptions, options, optionValues) 2)'

228  

229  

230cdef CUresult cuModuleLoadFatBinary(CUmodule* module, const void* fatCubin) except ?CUDA_ERROR_NOT_FOUND nogil: 

231 return _driver._cuModuleLoadFatBinary(module, fatCubin) 

232  

233  

234cdef CUresult cuModuleUnload(CUmodule hmod) except ?CUDA_ERROR_NOT_FOUND nogil: 

235 return _driver._cuModuleUnload(hmod) 2AbBb-d.d/d^b:d;dEbFb{d|d}d~d_baebe

236  

237  

238cdef CUresult cuModuleGetLoadingMode(CUmoduleLoadingMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil: 

239 return _driver._cuModuleGetLoadingMode(mode) 

240  

241  

242cdef CUresult cuModuleGetFunction(CUfunction* hfunc, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

243 return _driver._cuModuleGetFunction(hfunc, hmod, name) 2AbBb-d.d/d^b:d;dEbFb{d|d}d~d_baebe

244  

245  

246cdef CUresult cuModuleGetFunctionCount(unsigned int* count, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil: 

247 return _driver._cuModuleGetFunctionCount(count, mod) 2Ps

248  

249  

250cdef CUresult cuModuleEnumerateFunctions(CUfunction* functions, unsigned int numFunctions, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil: 

251 return _driver._cuModuleEnumerateFunctions(functions, numFunctions, mod) 

252  

253  

254cdef CUresult cuModuleGetGlobal(CUdeviceptr* dptr, size_t* bytes, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

255 return _driver._cuModuleGetGlobal_v2(dptr, bytes, hmod, name) 2^b_b

256  

257  

258cdef CUresult cuLinkCreate(unsigned int numOptions, CUjit_option* options, void** optionValues, CUlinkState* stateOut) except ?CUDA_ERROR_NOT_FOUND nogil: 

259 return _driver._cuLinkCreate_v2(numOptions, options, optionValues, stateOut) 

260  

261  

262cdef CUresult cuLinkAddData(CUlinkState state, CUjitInputType type, void* data, size_t size, const char* name, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil: 

263 return _driver._cuLinkAddData_v2(state, type, data, size, name, numOptions, options, optionValues) 

264  

265  

266cdef CUresult cuLinkAddFile(CUlinkState state, CUjitInputType type, const char* path, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil: 

267 return _driver._cuLinkAddFile_v2(state, type, path, numOptions, options, optionValues) 

268  

269  

270cdef CUresult cuLinkComplete(CUlinkState state, void** cubinOut, size_t* sizeOut) except ?CUDA_ERROR_NOT_FOUND nogil: 

271 return _driver._cuLinkComplete(state, cubinOut, sizeOut) 

272  

273  

274cdef CUresult cuLinkDestroy(CUlinkState state) except ?CUDA_ERROR_NOT_FOUND nogil: 

275 return _driver._cuLinkDestroy(state) 

276  

277  

278cdef CUresult cuModuleGetTexRef(CUtexref* pTexRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

279 return _driver._cuModuleGetTexRef(pTexRef, hmod, name) 

280  

281  

282cdef CUresult cuModuleGetSurfRef(CUsurfref* pSurfRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

283 return _driver._cuModuleGetSurfRef(pSurfRef, hmod, name) 

284  

285  

286cdef CUresult cuLibraryLoadData(CUlibrary* library, const void* code, CUjit_option* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, CUlibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?CUDA_ERROR_NOT_FOUND nogil: 

287 return _driver._cuLibraryLoadData(library, code, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 2`l

288  

289  

290cdef CUresult cuLibraryLoadFromFile(CUlibrary* library, const char* fileName, CUjit_option* jitOptions, void** jitOptionsValues, unsigned int numJitOptions, CUlibraryOption* libraryOptions, void** libraryOptionValues, unsigned int numLibraryOptions) except ?CUDA_ERROR_NOT_FOUND nogil: 

291 return _driver._cuLibraryLoadFromFile(library, fileName, jitOptions, jitOptionsValues, numJitOptions, libraryOptions, libraryOptionValues, numLibraryOptions) 

292  

293  

294cdef CUresult cuLibraryUnload(CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil: 

295 return _driver._cuLibraryUnload(library) 

296  

297  

298cdef CUresult cuLibraryGetKernel(CUkernel* pKernel, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

299 return _driver._cuLibraryGetKernel(pKernel, library, name) 2`l

300  

301  

302cdef CUresult cuLibraryGetKernelCount(unsigned int* count, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil: 

303 return _driver._cuLibraryGetKernelCount(count, lib) 

304  

305  

306cdef CUresult cuLibraryEnumerateKernels(CUkernel* kernels, unsigned int numKernels, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil: 

307 return _driver._cuLibraryEnumerateKernels(kernels, numKernels, lib) 

308  

309  

310cdef CUresult cuLibraryGetModule(CUmodule* pMod, CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil: 

311 return _driver._cuLibraryGetModule(pMod, library) 2Ps

312  

313  

314cdef CUresult cuKernelGetFunction(CUfunction* pFunc, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil: 

315 return _driver._cuKernelGetFunction(pFunc, kernel) 

316  

317  

318cdef CUresult cuKernelGetLibrary(CUlibrary* pLib, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil: 

319 return _driver._cuKernelGetLibrary(pLib, kernel) 

320  

321  

322cdef CUresult cuLibraryGetGlobal(CUdeviceptr* dptr, size_t* bytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

323 return _driver._cuLibraryGetGlobal(dptr, bytes, library, name) 

324  

325  

326cdef CUresult cuLibraryGetManaged(CUdeviceptr* dptr, size_t* bytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil: 

327 return _driver._cuLibraryGetManaged(dptr, bytes, library, name) 

328  

329  

330cdef CUresult cuLibraryGetUnifiedFunction(void** fptr, CUlibrary library, const char* symbol) except ?CUDA_ERROR_NOT_FOUND nogil: 

331 return _driver._cuLibraryGetUnifiedFunction(fptr, library, symbol) 

332  

333  

334cdef CUresult cuKernelGetAttribute(int* pi, CUfunction_attribute attrib, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

335 return _driver._cuKernelGetAttribute(pi, attrib, kernel, dev) 2owYlBc@!`lZx[!]!QsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s^!_!`!{!|!}!~!a#b#c#d#e#f#g#h#i#

336  

337  

338cdef CUresult cuKernelSetAttribute(CUfunction_attribute attrib, int val, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

339 return _driver._cuKernelSetAttribute(attrib, val, kernel, dev) 

340  

341  

342cdef CUresult cuKernelSetCacheConfig(CUkernel kernel, CUfunc_cache config, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

343 return _driver._cuKernelSetCacheConfig(kernel, config, dev) 

344  

345  

346cdef CUresult cuKernelGetName(const char** name, CUkernel hfunc) except ?CUDA_ERROR_NOT_FOUND nogil: 

347 return _driver._cuKernelGetName(name, hfunc) 2*'

348  

349  

350cdef CUresult cuKernelGetParamInfo(CUkernel kernel, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil: 

351 return _driver._cuKernelGetParamInfo(kernel, paramIndex, paramOffset, paramSize) 2[ Ge0x1x2x3x4x5x6x7x8x9x+'

352  

353  

354cdef CUresult cuMemGetInfo(size_t* free, size_t* total) except ?CUDA_ERROR_NOT_FOUND nogil: 

355 return _driver._cuMemGetInfo_v2(free, total) 2He

356  

357  

358cdef CUresult cuMemAlloc(CUdeviceptr* dptr, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil: 

359 return _driver._cuMemAlloc_v2(dptr, bytesize) 2AbBbrmptn#M Jmo#Kmp#q#r#s#t#ggskLmMmtksVtVuVHeu#EbFbNmv#w#ukx#vkWhy#z#A#vVB#wVC#D#xVyVE#F#G#zVH#AVBVCVDVEVFVGVHVIVI#JVKVLVMVJ#NVOVK#L#OmZh0h1h}l~lCj

360  

361  

362cdef CUresult cuMemAllocPitch(CUdeviceptr* dptr, size_t* pPitch, size_t WidthInBytes, size_t Height, unsigned int ElementSizeBytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

363 return _driver._cuMemAllocPitch_v2(dptr, pPitch, WidthInBytes, Height, ElementSizeBytes) 

364  

365  

366cdef CUresult cuMemFree(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

367 return _driver._cuMemFree_v2(dptr) 2H ybI J X ?bY Z ( ) * e F g h i AbBbhgamve/jwk:j~ abwe;j$cbmCbcmdm=jigembb?jxk@j, - . cbyk[jzk]jAk^jBk_j`j{j|j}j~jakbkckNcOc/ jgkg: ; = lgmgCkDkngogpgqgrg!s#s$s%s's(s4l)s*s+s,s-sPm.s/srmxe7 dbeb{e=dEkFk?dGk|e@dHk}e[dIk[fPcsgtg0f1fJk]dKkLk^dMk~e_dNkGdHd2f3fugvg4f5fwgxgajptQmn#M Jmo#Kmp#q#r#s#t#ggskLmMmtksVtVuVRcDb? @ `dHeIdJdu#EbFbfbgbhbibNmv#w#ukx#vkWhdfy#eefeBlClz#A#vVB#wVC#D#xVyVE#F#G#zVH#AVBVCVDVEVFVGVHVIVI#JVKVLVMVJ#NVOVK#L#M#N#PVO#QVP#Q#RVSVR#S#T#TVU#UVVVWVXVYVZV0V1V2VV#3V4V5V6VW#7V8VX#Y#Om'lZh0h1h}l~lnVoVCj[ Z#fmgmhmimjmkmlmmmnmompmqmheieje|b}bjb%f'f(f)f*f+f,f-f.f/f:f;f=f?f@fkeDjEjFjGjHjIjJjKjLjMjNjOjPjQjRjSjTjUjVjWjXjYjZj0j1j2j3j4j5j6j7j8j9j!j#j$j%j'j(j)j*j0c+j,j-j

368  

369  

370cdef CUresult cuMemGetAddressRange(CUdeviceptr* pbase, size_t* psize, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

371 return _driver._cuMemGetAddressRange_v2(pbase, psize, dptr) 

372  

373  

374cdef CUresult cuMemAllocHost(void** pp, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil: 

375 return _driver._cuMemAllocHost_v2(pp, bytesize) 22 f G N sb` j k l m n o p q r s t u v w x y O z A B C D P Q R S kb} ' U V W d ~bpb@b[b]bGbHbIbacbcXfYfZfccdcec5c6cEcFcGcfcgchc7c8ce 9cleHcIcJcJbKbLb!c#cKc,dLcMbNbObicjcqbK L F c g h i kclcmelb0 zbMcveodpd~ abweqd$cCbrdbbsdtd, - . cbudvdwdxdydzdAdBdCdDdEdFdNcOc9V!V#V$V/ jgkg: ; qt= lgOkmgPkCkDkyengRmogpgqgrg7 dbeb_ ScDb? @ 6 `dcedeSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!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~mcjdjejfjgjhjijjjkjljmjnjfbgbhbibNmukvkcf?s@s0#1#%V2#'V3#4#(V)V5#6#7#*V8#+V,V-V.V/V:V;V=V?V9#@V[V]V^V!#_V`V##$#Om[ `b{b{V

376  

377  

378cdef CUresult cuMemFreeHost(void* p) except ?CUDA_ERROR_NOT_FOUND nogil: 

379 return _driver._cuMemFreeHost(p) 22 f G N sb` j k l m n o p q r s t u v w x y O z A B C D P Q R S kb} ' U V W d ~bpb@b[b]bGbHbIbacbcXfYfZfccdcec5c6cEcFcGcfcgchc7c8ce 9cleHcIcJcJbKbLb!c#cKc,dLcMbNbObicjcqbK L F c g h i kclcmelb0 zbMcve/j:j~ abwe;j$cCb=jbb?j@j, - . cb[j]j^j_j`j{j|j}j~jakbkckNcOc9V!V#V$V/ jgkg: ; qt= lgOkmgPkCkDkyengRmogpgqgrg7 dbeb%#'#_ ScDb? @ 6 `dcedeSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!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~mcjdjejfjgjhjijjjkjljmjnjfbgbhbibNmukvkcf?s@s0#1#%V2#'V3#4#(V)V5#6#7#*V8#+V,V-V.V/V:V;V=V?V9#@V[V]V^V!#_V`V##$#Om[ `b{b{V

380  

381  

382cdef CUresult cuMemHostAlloc(void** pp, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

383 return _driver._cuMemHostAlloc(pp, bytesize, Flags) 2%#'#

384  

385  

386cdef CUresult cuMemHostGetDevicePointer(CUdeviceptr* pdptr, void* p, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

387 return _driver._cuMemHostGetDevicePointer_v2(pdptr, p, Flags) 

388  

389  

390cdef CUresult cuMemHostGetFlags(unsigned int* pFlags, void* p) except ?CUDA_ERROR_NOT_FOUND nogil: 

391 return _driver._cuMemHostGetFlags(pFlags, p) 

392  

393  

394cdef CUresult cuMemAllocManaged(CUdeviceptr* dptr, size_t bytesize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

395 return _driver._cuMemAllocManaged(dptr, bytesize, flags) 2H ybI J X ?bY Z ( ) * hgvewk~ abigbbxk, - . cbykzkAkBk/ jgkg: ; = lgmgCkDkngogpgqgrg9k!k$k'k)k*k4lmhnh,kohphPm-k.kxe7 dbeb{e=dEkFk?dGk|e@dHk}e[dIk[fPcsgtg0f1fJk]dKkLk^dMk~e_dNkGdHd2f3fugvg4f5fwgxgajQm`dIdJdNmukvkdfBlClM#N#PVO#QVP#Q#RVSVR#S#T#TVU#UVVVWVXVYVZV0V1V2VV#3V4V5V6VW#7V8VX#Y#Om'l

396  

397  

398cdef CUresult cuDeviceRegisterAsyncNotification(CUdevice device, CUasyncCallback callbackFunc, void* userData, CUasyncCallbackHandle* callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

399 return _driver._cuDeviceRegisterAsyncNotification(device, callbackFunc, userData, callback) 

400  

401  

402cdef CUresult cuDeviceUnregisterAsyncNotification(CUdevice device, CUasyncCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

403 return _driver._cuDeviceUnregisterAsyncNotification(device, callback) 

404  

405  

406cdef CUresult cuDeviceGetByPCIBusId(CUdevice* dev, const char* pciBusId) except ?CUDA_ERROR_NOT_FOUND nogil: 

407 return _driver._cuDeviceGetByPCIBusId(dev, pciBusId) 

408  

409  

410cdef CUresult cuDeviceGetPCIBusId(char* pciBusId, int len, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

411 return _driver._cuDeviceGetPCIBusId(pciBusId, len, dev) 

412  

413  

414cdef CUresult cuIpcGetEventHandle(CUipcEventHandle* pHandle, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

415 return _driver._cuIpcGetEventHandle(pHandle, event) 27 dbeb(#)#*#+#,#-#.#/#:#dV=h?h

416  

417  

418cdef CUresult cuIpcOpenEventHandle(CUevent* phEvent, CUipcEventHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil: 

419 return _driver._cuIpcOpenEventHandle(phEvent, handle) 

420  

421  

422cdef CUresult cuIpcGetMemHandle(CUipcMemHandle* pHandle, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

423 return _driver._cuIpcGetMemHandle(pHandle, dptr) 

424  

425  

426cdef CUresult cuIpcOpenMemHandle(CUdeviceptr* pdptr, CUipcMemHandle handle, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

427 return _driver._cuIpcOpenMemHandle_v2(pdptr, handle, Flags) 

428  

429  

430cdef CUresult cuIpcCloseMemHandle(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

431 return _driver._cuIpcCloseMemHandle(dptr) 

432  

433  

434cdef CUresult cuMemHostRegister(void* p, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

435 return _driver._cuMemHostRegister_v2(p, bytesize, Flags) 2DlEl

436  

437  

438cdef CUresult cuMemHostUnregister(void* p) except ?CUDA_ERROR_NOT_FOUND nogil: 

439 return _driver._cuMemHostUnregister(p) 2DlEl

440  

441  

442cdef CUresult cuMemcpy(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

443 return _driver._cuMemcpy(dst, src, ByteCount) 

444  

445  

446cdef CUresult cuMemcpyPeer(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

447 return _driver._cuMemcpyPeer(dstDevice, dstContext, srcDevice, srcContext, ByteCount) 

448  

449  

450cdef CUresult cuMemcpyHtoD(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

451 return _driver._cuMemcpyHtoD_v2(dstDevice, srcHost, ByteCount) 2ptM sVtVuV

452  

453  

454cdef CUresult cuMemcpyDtoH(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

455 return _driver._cuMemcpyDtoH_v2(dstHost, srcDevice, ByteCount) 23 4 5 9 ubT ! # E $ % vbwbxb)cmb*cfgImrkteueptM genbWcXc!f$f

456  

457  

458cdef CUresult cuMemcpyDtoD(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

459 return _driver._cuMemcpyDtoD_v2(dstDevice, srcDevice, ByteCount) 

460  

461  

462cdef CUresult cuMemcpyDtoA(CUarray dstArray, size_t dstOffset, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

463 return _driver._cuMemcpyDtoA_v2(dstArray, dstOffset, srcDevice, ByteCount) 

464  

465  

466cdef CUresult cuMemcpyAtoD(CUdeviceptr dstDevice, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

467 return _driver._cuMemcpyAtoD_v2(dstDevice, srcArray, srcOffset, ByteCount) 

468  

469  

470cdef CUresult cuMemcpyHtoA(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

471 return _driver._cuMemcpyHtoA_v2(dstArray, dstOffset, srcHost, ByteCount) 

472  

473  

474cdef CUresult cuMemcpyAtoH(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

475 return _driver._cuMemcpyAtoH_v2(dstHost, srcArray, srcOffset, ByteCount) 

476  

477  

478cdef CUresult cuMemcpyAtoA(CUarray dstArray, size_t dstOffset, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

479 return _driver._cuMemcpyAtoA_v2(dstArray, dstOffset, srcArray, srcOffset, ByteCount) 

480  

481  

482cdef CUresult cuMemcpy2D(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil: 

483 return _driver._cuMemcpy2D_v2(pCopy) 

484  

485  

486cdef CUresult cuMemcpy2DUnaligned(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil: 

487 return _driver._cuMemcpy2DUnaligned_v2(pCopy) 

488  

489  

490cdef CUresult cuMemcpy3D(const CUDA_MEMCPY3D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil: 

491 return _driver._cuMemcpy3D_v2(pCopy) 

492  

493  

494cdef CUresult cuMemcpy3DPeer(const CUDA_MEMCPY3D_PEER* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil: 

495 return _driver._cuMemcpy3DPeer(pCopy) 

496  

497  

498cdef CUresult cuMemcpyAsync(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

499 return _driver._cuMemcpyAsync(dst, src, ByteCount, hStream) 2H ybI J X ?bY Z ( ) * e K L F c g h i hgwk~ abwe$cCbigbbxk, - . cbykzkAkBk/ : ; qt= CkDkyexe7 dbeb{e=dEkFk?dGk|e@dHk}e[dIk[fPcsgtg0f1fJk]dKkLk^dMk~e_dNkGdHd2f3fugvg4f5fwgxgDb? @ `dIdJdfbgbhbibukvk%lojyj[ `b{b

500  

501  

502cdef CUresult cuMemcpyPeerAsync(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

503 return _driver._cuMemcpyPeerAsync(dstDevice, dstContext, srcDevice, srcContext, ByteCount, hStream) 

504  

505  

506cdef CUresult cuMemcpyHtoDAsync(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

507 return _driver._cuMemcpyHtoDAsync_v2(dstDevice, srcHost, ByteCount, hStream) 2JmKmggLmMmtk

508  

509  

510cdef CUresult cuMemcpyDtoHAsync(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

511 return _driver._cuMemcpyDtoHAsync_v2(dstHost, srcDevice, ByteCount, hStream) 2AbBb^bJmKmggskLmMmEbFb_b

512  

513  

514cdef CUresult cuMemcpyDtoDAsync(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

515 return _driver._cuMemcpyDtoDAsync_v2(dstDevice, srcDevice, ByteCount, hStream) 

516  

517  

518cdef CUresult cuMemcpyHtoAAsync(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

519 return _driver._cuMemcpyHtoAAsync_v2(dstArray, dstOffset, srcHost, ByteCount, hStream) 

520  

521  

522cdef CUresult cuMemcpyAtoHAsync(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

523 return _driver._cuMemcpyAtoHAsync_v2(dstHost, srcArray, srcOffset, ByteCount, hStream) 

524  

525  

526cdef CUresult cuMemcpy2DAsync(const CUDA_MEMCPY2D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

527 return _driver._cuMemcpy2DAsync_v2(pCopy, hStream) 

528  

529  

530cdef CUresult cuMemcpy3DAsync(const CUDA_MEMCPY3D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

531 return _driver._cuMemcpy3DAsync_v2(pCopy, hStream) 2jbqVrVmt

532  

533  

534cdef CUresult cuMemcpy3DPeerAsync(const CUDA_MEMCPY3D_PEER* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

535 return _driver._cuMemcpy3DPeerAsync(pCopy, hStream) 

536  

537  

538cdef CUresult cuMemsetD8(CUdeviceptr dstDevice, unsigned char uc, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil: 

539 return _driver._cuMemsetD8_v2(dstDevice, uc, N) 2nt)cmbot*cfgImrkteueAjge1 nbWcXc!f$f

540  

541  

542cdef CUresult cuMemsetD16(CUdeviceptr dstDevice, unsigned short us, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil: 

543 return _driver._cuMemsetD16_v2(dstDevice, us, N) 

544  

545  

546cdef CUresult cuMemsetD32(CUdeviceptr dstDevice, unsigned int ui, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil: 

547 return _driver._cuMemsetD32_v2(dstDevice, ui, N) 

548  

549  

550cdef CUresult cuMemsetD2D8(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil: 

551 return _driver._cuMemsetD2D8_v2(dstDevice, dstPitch, uc, Width, Height) 

552  

553  

554cdef CUresult cuMemsetD2D16(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil: 

555 return _driver._cuMemsetD2D16_v2(dstDevice, dstPitch, us, Width, Height) 

556  

557  

558cdef CUresult cuMemsetD2D32(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil: 

559 return _driver._cuMemsetD2D32_v2(dstDevice, dstPitch, ui, Width, Height) 

560  

561  

562cdef CUresult cuMemsetD8Async(CUdeviceptr dstDevice, unsigned char uc, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

563 return _driver._cuMemsetD8Async(dstDevice, uc, N, hStream) 2ubT ! # E $ % H ybI J e K L F c g h i hgve$cig, - . / : ; = vVyVAVBVCVJVKV%V)V+V,V-V@V[VPVSVUVVVWV3V4V

564  

565  

566cdef CUresult cuMemsetD16Async(CUdeviceptr dstDevice, unsigned short us, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

567 return _driver._cuMemsetD16Async(dstDevice, us, N, hStream) 2wVDVEVFVLVMV'V.V/V:V]V^VQVXVYVZV5V6V

568  

569  

570cdef CUresult cuMemsetD32Async(CUdeviceptr dstDevice, unsigned int ui, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

571 return _driver._cuMemsetD32Async(dstDevice, ui, N, hStream) 2xVzVGVHVIVNVOV(V*V;V=V?V_V`VRVTV0V1V2V7V8V

572  

573  

574cdef CUresult cuMemsetD2D8Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

575 return _driver._cuMemsetD2D8Async(dstDevice, dstPitch, uc, Width, Height, hStream) 

576  

577  

578cdef CUresult cuMemsetD2D16Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

579 return _driver._cuMemsetD2D16Async(dstDevice, dstPitch, us, Width, Height, hStream) 

580  

581  

582cdef CUresult cuMemsetD2D32Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

583 return _driver._cuMemsetD2D32Async(dstDevice, dstPitch, ui, Width, Height, hStream) 

584  

585  

586cdef CUresult cuArrayCreate(CUarray* pHandle, const CUDA_ARRAY_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

587 return _driver._cuArrayCreate_v2(pHandle, pAllocateArray) 2;#

588  

589  

590cdef CUresult cuArrayGetDescriptor(CUDA_ARRAY_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

591 return _driver._cuArrayGetDescriptor_v2(pArrayDescriptor, hArray) 

592  

593  

594cdef CUresult cuArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUarray array) except ?CUDA_ERROR_NOT_FOUND nogil: 

595 return _driver._cuArrayGetSparseProperties(sparseProperties, array) 

596  

597  

598cdef CUresult cuMipmappedArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUmipmappedArray mipmap) except ?CUDA_ERROR_NOT_FOUND nogil: 

599 return _driver._cuMipmappedArrayGetSparseProperties(sparseProperties, mipmap) 

600  

601  

602cdef CUresult cuArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUarray array, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil: 

603 return _driver._cuArrayGetMemoryRequirements(memoryRequirements, array, device) 

604  

605  

606cdef CUresult cuMipmappedArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUmipmappedArray mipmap, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil: 

607 return _driver._cuMipmappedArrayGetMemoryRequirements(memoryRequirements, mipmap, device) 

608  

609  

610cdef CUresult cuArrayGetPlane(CUarray* pPlaneArray, CUarray hArray, unsigned int planeIdx) except ?CUDA_ERROR_NOT_FOUND nogil: 

611 return _driver._cuArrayGetPlane(pPlaneArray, hArray, planeIdx) 

612  

613  

614cdef CUresult cuArrayDestroy(CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

615 return _driver._cuArrayDestroy(hArray) 2;#

616  

617  

618cdef CUresult cuArray3DCreate(CUarray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

619 return _driver._cuArray3DCreate_v2(pHandle, pAllocateArray) 

620  

621  

622cdef CUresult cuArray3DGetDescriptor(CUDA_ARRAY3D_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

623 return _driver._cuArray3DGetDescriptor_v2(pArrayDescriptor, hArray) 2l#m#mt

624  

625  

626cdef CUresult cuMipmappedArrayCreate(CUmipmappedArray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc, unsigned int numMipmapLevels) except ?CUDA_ERROR_NOT_FOUND nogil: 

627 return _driver._cuMipmappedArrayCreate(pHandle, pMipmappedArrayDesc, numMipmapLevels) 

628  

629  

630cdef CUresult cuMipmappedArrayGetLevel(CUarray* pLevelArray, CUmipmappedArray hMipmappedArray, unsigned int level) except ?CUDA_ERROR_NOT_FOUND nogil: 

631 return _driver._cuMipmappedArrayGetLevel(pLevelArray, hMipmappedArray, level) 

632  

633  

634cdef CUresult cuMipmappedArrayDestroy(CUmipmappedArray hMipmappedArray) except ?CUDA_ERROR_NOT_FOUND nogil: 

635 return _driver._cuMipmappedArrayDestroy(hMipmappedArray) 

636  

637  

638cdef CUresult cuMemGetHandleForAddressRange(void* handle, CUdeviceptr dptr, size_t size, CUmemRangeHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

639 return _driver._cuMemGetHandleForAddressRange(handle, dptr, size, handleType, flags) 

640  

641  

642cdef CUresult cuMemBatchDecompressAsync(CUmemDecompressParams* paramsArray, size_t count, unsigned int flags, size_t* errorIndex, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil: 

643 return _driver._cuMemBatchDecompressAsync(paramsArray, count, flags, errorIndex, stream) 

644  

645  

646cdef CUresult cuMemAddressReserve(CUdeviceptr* ptr, size_t size, size_t alignment, CUdeviceptr addr, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

647 return _driver._cuMemAddressReserve(ptr, size, alignment, addr, flags) 2mbfgtezj1 WcXc_l

648  

649  

650cdef CUresult cuMemAddressFree(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil: 

651 return _driver._cuMemAddressFree(ptr, size) 2mbfgte]l^lzj1 nbWcXc_lYcZc

652  

653  

654cdef CUresult cuMemCreate(CUmemGenericAllocationHandle* handle, size_t size, const CUmemAllocationProp* prop, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

655 return _driver._cuMemCreate(handle, size, prop, flags) 11

656  

657  

658cdef CUresult cuMemRelease(CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil: 

659 return _driver._cuMemRelease(handle) 2ue1

660  

661  

662cdef CUresult cuMemMap(CUdeviceptr ptr, size_t size, size_t offset, CUmemGenericAllocationHandle handle, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

663 return _driver._cuMemMap(ptr, size, offset, handle, flags) 11

664  

665  

666cdef CUresult cuMemMapArrayAsync(CUarrayMapInfo* mapInfoList, unsigned int count, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

667 return _driver._cuMemMapArrayAsync(mapInfoList, count, hStream) 

668  

669  

670cdef CUresult cuMemUnmap(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil: 

671 return _driver._cuMemUnmap(ptr, size) 11

672  

673  

674cdef CUresult cuMemSetAccess(CUdeviceptr ptr, size_t size, const CUmemAccessDesc* desc, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

675 return _driver._cuMemSetAccess(ptr, size, desc, count) 11

676  

677  

678cdef CUresult cuMemGetAccess(unsigned long long* flags, const CUmemLocation* location, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

679 return _driver._cuMemGetAccess(flags, location, ptr) 2ge

680  

681  

682cdef CUresult cuMemExportToShareableHandle(void* shareableHandle, CUmemGenericAllocationHandle handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

683 return _driver._cuMemExportToShareableHandle(shareableHandle, handle, handleType, flags) 2|V}V~Veb:s;saWbWcWdWeWfWEkGkHkIk0f1fKkMkNknt)cmb=#ot?#*cfggWImrktehW@#~iue2f3f4f5f

684  

685  

686cdef CUresult cuMemImportFromShareableHandle(CUmemGenericAllocationHandle* handle, void* osHandle, CUmemAllocationHandleType shHandleType) except ?CUDA_ERROR_NOT_FOUND nogil: 

687 return _driver._cuMemImportFromShareableHandle(handle, osHandle, shHandleType) 

688  

689  

690cdef CUresult cuMemGetAllocationGranularity(size_t* granularity, const CUmemAllocationProp* prop, CUmemAllocationGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil: 

691 return _driver._cuMemGetAllocationGranularity(granularity, prop, option) 2:bCcd!|V}V~Veb:s;saWbWcWdWeWfWEkGkHkIk0f1fKkMkNknt)cmb=#ot?#*cfggWImrkte,'hW@#~iue2f3f4f5f]l^lzjJsTcKsLsAjge6f7f8fUcVc9fMs1 nbWcXc!fBj_lXxCjNsYcZcOs$f

692  

693  

694cdef CUresult cuMemGetAllocationPropertiesFromHandle(CUmemAllocationProp* prop, CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil: 

695 return _driver._cuMemGetAllocationPropertiesFromHandle(prop, handle) 2)cmb*cgWrktehWue

696  

697  

698cdef CUresult cuMemRetainAllocationHandle(CUmemGenericAllocationHandle* handle, void* addr) except ?CUDA_ERROR_NOT_FOUND nogil: 

699 return _driver._cuMemRetainAllocationHandle(handle, addr) 2mbue]l^lzj1 nbYcZc

700  

701  

702cdef CUresult cuMemFreeAsync(CUdeviceptr dptr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

703 return _driver._cuMemFreeAsync(dptr, hStream) 2rtWt

704  

705  

706cdef CUresult cuMemAllocAsync(CUdeviceptr* dptr, size_t bytesize, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

707 return _driver._cuMemAllocAsync(dptr, bytesize, hStream) 

708  

709  

710cdef CUresult cuMemPoolTrimTo(CUmemoryPool pool, size_t minBytesToKeep) except ?CUDA_ERROR_NOT_FOUND nogil: 

711 return _driver._cuMemPoolTrimTo(pool, minBytesToKeep) 

712  

713  

714cdef CUresult cuMemPoolSetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

715 return _driver._cuMemPoolSetAttribute(pool, attr, value) 2stQc

716  

717  

718cdef CUresult cuMemPoolGetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

719 return _driver._cuMemPoolGetAttribute(pool, attr, value) 2+btb| ubT =bSfTf! # E Uf$ % vbwbVfWfxbldmdndQkRkSkEeFeanbncnH ybI J X ?bY Z e K L c g h i ;eodpd~ abqd=eCb?e@erd[ebbsdtdcbudvdwdxdydzdAdBdCdDdEdFdNcOc/ pw[#~istQcRcDb? @ fbgbhbibeefe]#nsos7vrt^#iWpjws0i*lHfxs1iys2izs3iAs4i+lIfBs5i,lrj-l.l/l:lsj;lCs6itj9dDs7iEs8iFs9iGs!iuj!dHs#iUl=lIs?lvjwj@l.j#f[ `b{b2h4h!h$h,hb [h}hfimitiAiHiOiheieje|b}bjb%f'f(f)f*f+f,f-f.f/f:f;f=f?f@fkeDjEjFjGjHjIjJjKjLjMjNjOjPjQjRjSjTjUjVjWjXjYjZj0j1j2j3j4j5j6j7j8j9j!j#j$j%j'j(j)j*j0c+j,j-j

720  

721  

722cdef CUresult cuMemPoolSetAccess(CUmemoryPool pool, const CUmemAccessDesc* map, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

723 return _driver._cuMemPoolSetAccess(pool, map, count) 

724  

725  

726cdef CUresult cuMemPoolGetAccess(CUmemAccess_flags* flags, CUmemoryPool memPool, CUmemLocation* location) except ?CUDA_ERROR_NOT_FOUND nogil: 

727 return _driver._cuMemPoolGetAccess(flags, memPool, location) 2iW

728  

729  

730cdef CUresult cuMemPoolCreate(CUmemoryPool* pool, const CUmemPoolProps* poolProps) except ?CUDA_ERROR_NOT_FOUND nogil: 

731 return _driver._cuMemPoolCreate(pool, poolProps) 2stay

732  

733  

734cdef CUresult cuMemPoolDestroy(CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil: 

735 return _driver._cuMemPoolDestroy(pool) 2stay

736  

737  

738cdef CUresult cuMemAllocFromPoolAsync(CUdeviceptr* dptr, size_t bytesize, CUmemoryPool pool, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

739 return _driver._cuMemAllocFromPoolAsync(dptr, bytesize, pool, hStream) 2rt

740  

741  

742cdef CUresult cuMemPoolExportToShareableHandle(void* handle_out, CUmemoryPool pool, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

743 return _driver._cuMemPoolExportToShareableHandle(handle_out, pool, handleType, flags) 2]kqhtt^kutrh_ksh`kth{k|kvtuh-'}kvhxe~kwh.'alxhclyhelzhflAhglhliljlklllmlnlolplqlrlBhChDhEhFhGhHhIhJhKhLhMhslNhtlOhulPhvlQhwlRhsgtgxlShylThzlUhGdHdugvgwgxg0iHf1i2i3i4iIf5i6i9d7i8i9i!i!d#iJf_r`rL!M!N!O!kflf

744  

745  

746cdef CUresult cuMemPoolImportFromShareableHandle(CUmemoryPool* pool_out, void* handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

747 return _driver._cuMemPoolImportFromShareableHandle(pool_out, handle, handleType, flags) 

748  

749  

750cdef CUresult cuMemPoolExportPointer(CUmemPoolPtrExportData* shareData_out, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

751 return _driver._cuMemPoolExportPointer(shareData_out, ptr) 2ttut8n5ljW6l{kvtxe7 dbbl|idl}ikWlWmWnWoWpW7l8l9l!l#l$l{e=dFk?d|e@d}e[d[fPcsgtgJk]dLk^d~e_dGdHdugvgwgxgJfkflf

752  

753  

754cdef CUresult cuMemPoolImportPointer(CUdeviceptr* ptr_out, CUmemoryPool pool, CUmemPoolPtrExportData* shareData) except ?CUDA_ERROR_NOT_FOUND nogil: 

755 return _driver._cuMemPoolImportPointer(ptr_out, pool, shareData) 

756  

757  

758cdef CUresult cuMulticastCreate(CUmemGenericAllocationHandle* mcHandle, const CUmulticastObjectProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil: 

759 return _driver._cuMulticastCreate(mcHandle, prop) 

760  

761  

762cdef CUresult cuMulticastAddDevice(CUmemGenericAllocationHandle mcHandle, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

763 return _driver._cuMulticastAddDevice(mcHandle, dev) 

764  

765  

766cdef CUresult cuMulticastBindMem(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUmemGenericAllocationHandle memHandle, size_t memOffset, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

767 return _driver._cuMulticastBindMem(mcHandle, mcOffset, memHandle, memOffset, size, flags) 

768  

769  

770cdef CUresult cuMulticastBindAddr(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

771 return _driver._cuMulticastBindAddr(mcHandle, mcOffset, memptr, size, flags) 

772  

773  

774cdef CUresult cuMulticastUnbind(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil: 

775 return _driver._cuMulticastUnbind(mcHandle, dev, mcOffset, size) 

776  

777  

778cdef CUresult cuMulticastGetGranularity(size_t* granularity, const CUmulticastObjectProp* prop, CUmulticastGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil: 

779 return _driver._cuMulticastGetGranularity(granularity, prop, option) 

780  

781  

782cdef CUresult cuPointerGetAttribute(void* data, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

783 return _driver._cuPointerGetAttribute(data, attribute, ptr) 23 4 5 9 TbUbVbWbXbYb+btb{ kb| :b=b! # E $ Cc% GbHbIbccdcecfcgchce 9cJbKbLbMbNbObK L F c kclcmexeQm6 Zb0b1bb 2b3b4b5b6b7b8b9b|b}bke0c

784  

785  

786cdef CUresult cuMemPrefetchAsync(CUdeviceptr devPtr, size_t count, CUmemLocation location, unsigned int flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

787 return _driver._cuMemPrefetchAsync_v2(devPtr, count, location, flags, hStream) 2wtxtseytztAtBt

788  

789  

790cdef CUresult cuMemAdvise(CUdeviceptr devPtr, size_t count, CUmem_advise advice, CUmemLocation location) except ?CUDA_ERROR_NOT_FOUND nogil: 

791 return _driver._cuMemAdvise_v2(devPtr, count, advice, location) 23nlh#k%k(k_#PmqWrWaj

792  

793  

794cdef CUresult cuMemRangeGetAttribute(void* data, size_t dataSize, CUmem_range_attribute attribute, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

795 return _driver._cuMemRangeGetAttribute(data, dataSize, attribute, devPtr, count) 2Tk3nlh#k%k(kseytzt/'AtBtPmqWrWdnenaj

796  

797  

798cdef CUresult cuMemRangeGetAttributes(void** data, size_t* dataSizes, CUmem_range_attribute* attributes, size_t numAttributes, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

799 return _driver._cuMemRangeGetAttributes(data, dataSizes, attributes, numAttributes, devPtr, count) 2aj

800  

801  

802cdef CUresult cuPointerSetAttribute(const void* value, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

803 return _driver._cuPointerSetAttribute(value, attribute, ptr) 2Qm

804  

805  

806cdef CUresult cuPointerGetAttributes(unsigned int numAttributes, CUpointer_attribute* attributes, void** data, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

807 return _driver._cuPointerGetAttributes(numAttributes, attributes, data, ptr) 22 f G N sb` j k l m n o p q r s t u v w x y O z A B C D P Q R S } ' U V W d ~b0 zbMcfnTk3nlh#k%k(k_#wtxtseytztAtBt1!2!PmqWrWdnenrmQm:'GmHmDb? @ cedeSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!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~mcjdjejfjgjhjijjjkjljmjnjfbgbhbibcfdfeefe;'BlCl?s@sDlEl'lps@l[l[ `b{b|b}bke='?'@'[']'^'_'`'{'|'}'

808  

809  

810cdef CUresult cuStreamCreate(CUstream* phStream, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

811 return _driver._cuStreamCreate(phStream, Flags) 2AbBb-d.d/d^b:d;dzesW%cncM ggsktk`#EbFb{d|d}d~d_baebe

812  

813  

814cdef CUresult cuStreamCreateWithPriority(CUstream* phStream, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil: 

815 return _driver._cuStreamCreateWithPriority(phStream, flags, priority) 

816  

817  

818cdef CUresult cuStreamGetPriority(CUstream hStream, int* priority) except ?CUDA_ERROR_NOT_FOUND nogil: 

819 return _driver._cuStreamGetPriority(hStream, priority) 2pV

820  

821  

822cdef CUresult cuStreamGetDevice(CUstream hStream, CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil: 

823 return _driver._cuStreamGetDevice(hStream, device) 

824  

825  

826cdef CUresult cuStreamGetFlags(CUstream hStream, unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

827 return _driver._cuStreamGetFlags(hStream, flags) 2pV

828  

829  

830cdef CUresult cuStreamGetId(CUstream hStream, unsigned long long* streamId) except ?CUDA_ERROR_NOT_FOUND nogil: 

831 return _driver._cuStreamGetId(hStream, streamId) 

832  

833  

834cdef CUresult cuStreamGetCtx(CUstream hStream, CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

835 return _driver._cuStreamGetCtx(hStream, pctx) 23l5l6l|i}i7l8l9l!l#l$l=d?d@d[dPc]d^d_dVh=sqjtj9duj!dwj[lxjyjJfRx

836  

837  

838cdef CUresult cuStreamGetCtx_v2(CUstream hStream, CUcontext* pCtx, CUgreenCtx* pGreenCtx) except ?CUDA_ERROR_NOT_FOUND nogil: 

839 return _driver._cuStreamGetCtx_v2(hStream, pCtx, pGreenCtx) 

840  

841  

842cdef CUresult cuStreamWaitEvent(CUstream hStream, CUevent hEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

843 return _driver._cuStreamWaitEvent(hStream, hEvent, Flags) 2dk#d$drb%dRb'cj k l m n o p q r s t u v w x y z A B C D + lt0c

844  

845  

846cdef CUresult cuStreamAddCallback(CUstream hStream, CUstreamCallback callback, void* userData, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

847 return _driver._cuStreamAddCallback(hStream, callback, userData, flags) 

848  

849  

850cdef CUresult cuStreamBeginCapture(CUstream hStream, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil: 

851 return _driver._cuStreamBeginCapture_v2(hStream, mode) 27dDgEgxm[sdkBeCeDe]sKf^s^f_f`f{f_s2 $i#df neG %i`s$ducN vc{srbLf|s%dRb'csbwcMf'iym` j k l m n o p q r s t u v w x y O z A B C D P Q R S 8 ldmdndQkRkSkEeFeanbncnCtDtEtH I J X Y Z ( ) * ygzgAgocpcqce F c g h i 0 zb]i^i_i`i(c{i+ tWuWOkPkyenc6f7f8f9fYcZcjb

852  

853  

854cdef CUresult cuStreamBeginCaptureToGraph(CUstream hStream, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil: 

855 return _driver._cuStreamBeginCaptureToGraph(hStream, hGraph, dependencies, dependencyData, numDependencies, mode) 2f nej k l m n o p q r s t u v w x y O z A B C D P Q R S 0 +

856  

857  

858cdef CUresult cuThreadExchangeStreamCaptureMode(CUstreamCaptureMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil: 

859 return _driver._cuThreadExchangeStreamCaptureMode(mode) 2+btb| ubT =bSfTf! # E Uf$ % vbwbVfWfxbldmdndQkRkSkEeFeanbncnH ybI J X ?bY Z e K L c g h i ;eodpd~ abqd=eCb?e@erd[ebbsdtdcbudvdwdxdydzdAdBdCdDdEdFdNcOc/ pw[#~iQcRcDb? @ fbgbhbibeefe]#nsos7v^#iWpj@l#f[ `b{b2h4h!h$h,hb [h}hfimitiAiHiOiheieje|b}bjb%f'f(f)f*f+f,f-f.f/f:f;f=f?f@fkeDjEjFjGjHjIjJjKjLjMjNjOjPjQjRjSjTjUjVjWjXjYjZj0j1j2j3j4j5j6j7j8j9j!j#j$j%j'j(j)j*j0c+j,j-j

860  

861  

862cdef CUresult cuStreamEndCapture(CUstream hStream, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

863 return _driver._cuStreamEndCapture(hStream, phGraph) 27dDgEgxm[sdkBeCeDe]sKf^s^f_f`f{f_s2 $i#df neG %i`s$ducN vc{srbLf|s%dRb'csbwcMf'iym` j k l m n o p q r s t u v w x y O z A B C D P Q R S 8 ldmdndQkRkSkEeFeanbncnCtDtEtH I J X Y Z ( ) * ygzgAgocpcqce F c g h i 0 zb]i^i_i`i(c{i+ tWuWOkPkyenc6f7f8f9fYcZcjb

864  

865  

866cdef CUresult cuStreamIsCapturing(CUstream hStream, CUstreamCaptureStatus* captureStatus) except ?CUDA_ERROR_NOT_FOUND nogil: 

867 return _driver._cuStreamIsCapturing(hStream, captureStatus) 2+btb| ubT =bSfTf! # E Uf$ % vbwbVfWfxbQkRkSkCtDtEtH ybI J X ?bY Z ( ) * ygzgAgocpcqce K L c g h i ls2l3l;eodpd~ abweqd$c=eCb?e@erd[ebbsdtd, - . cbudvdwdxdydzdAdBdCdDdEdFdNcOc/ : ; = fnTk~']ese^e_e`ednena(b(c(d(e(ttut8n5ljW6l{kvtxe7 dbbl|idl}ikWlWmWnWoWpW7l8l9l!l#l$l{e=dFk?d|e@d}e[d[fPcsgtgJk]dLk^d~e_d~iGdHdugvgwgxgQcRc{l|l8sDb? @ fbgbhbibeefensos%lps(lojpj)lqj*lHf+lIfrjsjtj9duj!d?lvjwjf(@l[lxjyjJfRx.j#f[ `b{b2h4h!h$h,hb kflf[h}hfimitiAiHiOiheieje|b}bjb%f'f(f)f*f+f,f-f.f/f:f;f=f?f@fkeDjEjFjGjHjIjJjKjLjMjNjOjPjQjRjSjTjUjVjWjXjYjZj0j1j2j3j4j5j6j7j8j9j!j#j$j%j'j(j)j*j0c+j,j-j

868  

869  

870cdef CUresult cuStreamGetCaptureInfo_v2(CUstream hStream, CUstreamCaptureStatus* captureStatus_out, cuuint64_t* id_out, CUgraph* graph_out, const CUgraphNode** dependencies_out, size_t* numDependencies_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

871 return _driver._cuStreamGetCaptureInfo_v2(hStream, captureStatus_out, id_out, graph_out, dependencies_out, numDependencies_out) 

872  

873  

874cdef CUresult cuStreamGetCaptureInfo(CUstream hStream, CUstreamCaptureStatus* captureStatus_out, cuuint64_t* id_out, CUgraph* graph_out, const CUgraphNode** dependencies_out, const CUgraphEdgeData** edgeData_out, size_t* numDependencies_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

875 return _driver._cuStreamGetCaptureInfo_v3(hStream, captureStatus_out, id_out, graph_out, dependencies_out, edgeData_out, numDependencies_out) 2Y!7dDgEgZ!xm[sdkBeCeDe]sKf^s^f_f`f{f_s2 $i#df neG %i`s$ducN vc{srbLf|s%dRb'csbwcMf'iym` j k l m n o p q r s t u v w x y O z A B C D P Q R S 8 ldmdndQkRkSkEeFeanbncnCtDtEtH I J X Y Z ( ) * ygzgAgocpcqce F c g h i 0 zb]i^i_i`i(c{i+ hgvewk~ abwe$cCbtWuWigbbvWxk, - . cbykzkAkBkg(h(i(NcOc/ jgkg: ; = lgOkmgPkyengRmogpgqgrgTc6f7f8fUcVc9fYcZcjb

876  

877  

878cdef CUresult cuStreamUpdateCaptureDependencies(CUstream hStream, CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

879 return _driver._cuStreamUpdateCaptureDependencies_v2(hStream, dependencies, dependencyData, numDependencies, flags) 22 f neG j k l m n o p q r s t u v w x y O z A B C D P Q R S 8 0 +

880  

881  

882cdef CUresult cuStreamAttachMemAsync(CUstream hStream, CUdeviceptr dptr, size_t length, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

883 return _driver._cuStreamAttachMemAsync(hStream, dptr, length, flags) 

884  

885  

886cdef CUresult cuStreamQuery(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

887 return _driver._cuStreamQuery(hStream) 

888  

889  

890cdef CUresult cuStreamSynchronize(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

891 return _driver._cuStreamSynchronize(hStream) 27dBeCeDeKf^f_f`f{f2 f G N rbLfsbwcMf` j k l m n o p q r s t u v w x y O z A B C D P Q R S ekfkgkhkik'd(d)dNfxc|fjkkkOfPfQf*iRf3 4 5 9 (b)b*byc/i+bUiobCflkmktbmcnkkb| :bubT Bc;b=i=bSfTf! # E Uf$ Cc% vbwbVfWfxbDfok} ' U V W d ~b] H ybI J X ?bY Z ( ) * ygzgAgocpcqc8dpbPbagbgzmAm@b[b]bGbHbIbacbcXfYfZfccdcec5c6cEcFcGcfcgchc7c8cWie 9cleQbqerepkqkHcIcJcJbKbLb!c#cgn^ dgegEmFmKc,dLcMbNbObicjcEfqbK L F c g h i kclcmelbXiYiFfGf0 zbMcZiAbBb-d.d/d^b:d;dhgamve/jwk:j~ abwe;j$cbmCbcmdm=jigembbvW?jxk@j, - . cbyk[jzk]jAk^jBk_j`j{j|j}j~jakbkckNcOc9V!V#V$V/ jgkg: ; qt= lgOkmgPkCkDkyengRmogpgqgrgfnTkwtxt]eseytzt^eAtBt_e`ednenttut8n5l|VjW6l}V{kvt~Vxe7 dbebbl|i:sdl}i;sj(kWlWk(l(mWnWm(n(oWpWo(p(7l8lq(r(9l!ls(t(#l$lu(aWbWv(cWdWw(eWfWx({e=dEkFk?dGk|e@dHk}e[dIk[fPcsgtg0f1fJk]dKkLk^dMk~e_dNkGdHd2f3fugvg4f5fwgxgncM JmKmggskLmMmtkQcRcaf_ bfScDb? @ wW6 `dIdJdEbFb{d|d}d~d_baebeKdcedemsSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!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~mcjdjejfjgjhjijjjkjljmjnjfbgbhbibeeferty(.jnVoVTcUcVc1 #f[ `b{bZ#fmgmhmimjmkmlmmmnmompmqmk#ltheieje|b}bjb%fqVrVmt'f(f)f*f+f,f-f.f/f:f;f=f{V?f@fkeDjEjFjGjHjIjJjKjLjMjNjOjPjQjRjSjTjUjVjWjXjYjZj0j1j2j3j4j5j6j7j8j9j!j#j$j%j'j(j)j*j0c+j,j-j

892  

893  

894cdef CUresult cuStreamDestroy(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

895 return _driver._cuStreamDestroy_v2(hStream) 2AbBb-d.d/d^b:d;dzesW%cncM ggsktk`#EbFb{d|d}d~d_baebe

896  

897  

898cdef CUresult cuStreamCopyAttributes(CUstream dst, CUstream src) except ?CUDA_ERROR_NOT_FOUND nogil: 

899 return _driver._cuStreamCopyAttributes(dst, src) 

900  

901  

902cdef CUresult cuStreamGetAttribute(CUstream hStream, CUstreamAttrID attr, CUstreamAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

903 return _driver._cuStreamGetAttribute(hStream, attr, value_out) 

904  

905  

906cdef CUresult cuStreamSetAttribute(CUstream hStream, CUstreamAttrID attr, const CUstreamAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

907 return _driver._cuStreamSetAttribute(hStream, attr, value) 

908  

909  

910cdef CUresult cuEventCreate(CUevent* phEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

911 return _driver._cuEventCreate(phEvent, Flags) 2{#

912  

913  

914cdef CUresult cuEventRecord(CUevent hEvent, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

915 return _driver._cuEventRecord(hEvent, hStream) 2dk#d$drb%dRb'cj k l m n o p q r s t u v w x y z A B C D + 7 dbeb(#)#*#+#,#-#.#/#:#af_ bf3!4!5!6!7!8!Sc9!!!#!$!%!mVbtbjwWTcUcVcdV=h?hj#lt0c

916  

917  

918cdef CUresult cuEventRecordWithFlags(CUevent hEvent, CUstream hStream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

919 return _driver._cuEventRecordWithFlags(hEvent, hStream, flags) 

920  

921  

922cdef CUresult cuEventQuery(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

923 return _driver._cuEventQuery(hEvent) 2}s:i;iagqedgScmVbtTcUcVc

924  

925  

926cdef CUresult cuEventSynchronize(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

927 return _driver._cuEventSynchronize(hEvent) 2_ ScbtbjwW

928  

929  

930cdef CUresult cuEventDestroy(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

931 return _driver._cuEventDestroy_v2(hEvent) 2{#

932  

933  

934cdef CUresult cuEventElapsedTime(float* pMilliseconds, CUevent hStart, CUevent hEnd) except ?CUDA_ERROR_NOT_FOUND nogil: 

935 return _driver._cuEventElapsedTime_v2(pMilliseconds, hStart, hEnd) 2af_ bfbj

936  

937  

938cdef CUresult cuImportExternalMemory(CUexternalMemory* extMem_out, const CUDA_EXTERNAL_MEMORY_HANDLE_DESC* memHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

939 return _driver._cuImportExternalMemory(extMem_out, memHandleDesc) 

940  

941  

942cdef CUresult cuExternalMemoryGetMappedBuffer(CUdeviceptr* devPtr, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_BUFFER_DESC* bufferDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

943 return _driver._cuExternalMemoryGetMappedBuffer(devPtr, extMem, bufferDesc) 

944  

945  

946cdef CUresult cuExternalMemoryGetMappedMipmappedArray(CUmipmappedArray* mipmap, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC* mipmapDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

947 return _driver._cuExternalMemoryGetMappedMipmappedArray(mipmap, extMem, mipmapDesc) 

948  

949  

950cdef CUresult cuDestroyExternalMemory(CUexternalMemory extMem) except ?CUDA_ERROR_NOT_FOUND nogil: 

951 return _driver._cuDestroyExternalMemory(extMem) 

952  

953  

954cdef CUresult cuImportExternalSemaphore(CUexternalSemaphore* extSem_out, const CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC* semHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

955 return _driver._cuImportExternalSemaphore(extSem_out, semHandleDesc) 

956  

957  

958cdef CUresult cuSignalExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil: 

959 return _driver._cuSignalExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream) 

960  

961  

962cdef CUresult cuWaitExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil: 

963 return _driver._cuWaitExternalSemaphoresAsync(extSemArray, paramsArray, numExtSems, stream) 

964  

965  

966cdef CUresult cuDestroyExternalSemaphore(CUexternalSemaphore extSem) except ?CUDA_ERROR_NOT_FOUND nogil: 

967 return _driver._cuDestroyExternalSemaphore(extSem) 

968  

969  

970cdef CUresult cuStreamWaitValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

971 return _driver._cuStreamWaitValue32_v2(stream, addr, value, flags) 

972  

973  

974cdef CUresult cuStreamWaitValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

975 return _driver._cuStreamWaitValue64_v2(stream, addr, value, flags) 

976  

977  

978cdef CUresult cuStreamWriteValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

979 return _driver._cuStreamWriteValue32_v2(stream, addr, value, flags) 

980  

981  

982cdef CUresult cuStreamWriteValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

983 return _driver._cuStreamWriteValue64_v2(stream, addr, value, flags) 

984  

985  

986cdef CUresult cuStreamBatchMemOp(CUstream stream, unsigned int count, CUstreamBatchMemOpParams* paramArray, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

987 return _driver._cuStreamBatchMemOp_v2(stream, count, paramArray, flags) 

988  

989  

990cdef CUresult cuFuncGetAttribute(int* pi, CUfunction_attribute attrib, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil: 

991 return _driver._cuFuncGetAttribute(pi, attrib, hfunc) 

992  

993  

994cdef CUresult cuFuncSetAttribute(CUfunction hfunc, CUfunction_attribute attrib, int value) except ?CUDA_ERROR_NOT_FOUND nogil: 

995 return _driver._cuFuncSetAttribute(hfunc, attrib, value) 

996  

997  

998cdef CUresult cuFuncSetCacheConfig(CUfunction hfunc, CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil: 

999 return _driver._cuFuncSetCacheConfig(hfunc, config) 

1000  

1001  

1002cdef CUresult cuFuncGetModule(CUmodule* hmod, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil: 

1003 return _driver._cuFuncGetModule(hmod, hfunc) 

1004  

1005  

1006cdef CUresult cuFuncGetName(const char** name, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil: 

1007 return _driver._cuFuncGetName(name, hfunc) 2z(

1008  

1009  

1010cdef CUresult cuFuncGetParamInfo(CUfunction func, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil: 

1011 return _driver._cuFuncGetParamInfo(func, paramIndex, paramOffset, paramSize) 

1012  

1013  

1014cdef CUresult cuFuncIsLoaded(CUfunctionLoadingState* state, CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil: 

1015 return _driver._cuFuncIsLoaded(state, function) 

1016  

1017  

1018cdef CUresult cuFuncLoad(CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil: 

1019 return _driver._cuFuncLoad(function) 

1020  

1021  

1022cdef CUresult cuLaunchKernel(CUfunction f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, CUstream hStream, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil: 

1023 return _driver._cuLaunchKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams, extra) 2AbBb-d.d/d^b:d;dEbFb{d|d}d~d_baebe

1024  

1025  

1026cdef CUresult cuLaunchKernelEx(const CUlaunchConfig* config, CUfunction f, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil: 

1027 return _driver._cuLaunchKernelEx(config, f, kernelParams, extra) 2Kf2 $i#df G %i$ducN vcrbLf%dRbsbwcMf'i` j k l m n o p q r s t u v w x y O z A B C D P Q R S H ybI J X ?bY Z ( ) * 0 zb]i^i_i`i(c{i+ 7 dbeb_ ScbjDb? @ `dKdcedemsSmTmUmVmWmXmYmZm0m1m2m3m4m5m6m7m8m9m!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~mcjdjejfjgjhjijjjkjljmjnjfbgbhbibTcUcVc[ `b{b

1028  

1029  

1030cdef CUresult cuLaunchCooperativeKernel(CUfunction f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, CUstream hStream, void** kernelParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1031 return _driver._cuLaunchCooperativeKernel(f, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams) 

1032  

1033  

1034cdef CUresult cuLaunchCooperativeKernelMultiDevice(CUDA_LAUNCH_PARAMS* launchParamsList, unsigned int numDevices, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1035 return _driver._cuLaunchCooperativeKernelMultiDevice(launchParamsList, numDevices, flags) 

1036  

1037  

1038cdef CUresult cuLaunchHostFunc(CUstream hStream, CUhostFn fn, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil: 

1039 return _driver._cuLaunchHostFunc(hStream, fn, userData) 27d^f_f`f{f8 nc

1040  

1041  

1042cdef CUresult cuFuncSetBlockShape(CUfunction hfunc, int x, int y, int z) except ?CUDA_ERROR_NOT_FOUND nogil: 

1043 return _driver._cuFuncSetBlockShape(hfunc, x, y, z) 

1044  

1045  

1046cdef CUresult cuFuncSetSharedSize(CUfunction hfunc, unsigned int bytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1047 return _driver._cuFuncSetSharedSize(hfunc, bytes) 

1048  

1049  

1050cdef CUresult cuParamSetSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1051 return _driver._cuParamSetSize(hfunc, numbytes) 

1052  

1053  

1054cdef CUresult cuParamSeti(CUfunction hfunc, int offset, unsigned int value) except ?CUDA_ERROR_NOT_FOUND nogil: 

1055 return _driver._cuParamSeti(hfunc, offset, value) 

1056  

1057  

1058cdef CUresult cuParamSetf(CUfunction hfunc, int offset, float value) except ?CUDA_ERROR_NOT_FOUND nogil: 

1059 return _driver._cuParamSetf(hfunc, offset, value) 

1060  

1061  

1062cdef CUresult cuParamSetv(CUfunction hfunc, int offset, void* ptr, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1063 return _driver._cuParamSetv(hfunc, offset, ptr, numbytes) 

1064  

1065  

1066cdef CUresult cuLaunch(CUfunction f) except ?CUDA_ERROR_NOT_FOUND nogil: 

1067 return _driver._cuLaunch(f) 

1068  

1069  

1070cdef CUresult cuLaunchGrid(CUfunction f, int grid_width, int grid_height) except ?CUDA_ERROR_NOT_FOUND nogil: 

1071 return _driver._cuLaunchGrid(f, grid_width, grid_height) 

1072  

1073  

1074cdef CUresult cuLaunchGridAsync(CUfunction f, int grid_width, int grid_height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1075 return _driver._cuLaunchGridAsync(f, grid_width, grid_height, hStream) 

1076  

1077  

1078cdef CUresult cuParamSetTexRef(CUfunction hfunc, int texunit, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1079 return _driver._cuParamSetTexRef(hfunc, texunit, hTexRef) 

1080  

1081  

1082cdef CUresult cuFuncSetSharedMemConfig(CUfunction hfunc, CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil: 

1083 return _driver._cuFuncSetSharedMemConfig(hfunc, config) 

1084  

1085  

1086cdef CUresult cuGraphCreate(CUgraph* phGraph, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1087 return _driver._cuGraphCreate(phGraph, flags) 2gVhV{r|r(iFg0!GgsmVl}rWlOgIePgruJeQgRg)iA(B(ekfkgkhkikC(D(E(F(|#BgG(Cg'd(d)dNfxc|fjkkk^9_9OfPfQf*iRf3 4 5 9 (b)b*byc`9H(I(J(~rasbs+i,i-iUkVkWkXlcsSgTg+cKeLeMeNeRnSnUgVgOeTb,c-c.c/cWgXgYgZg:cPeQeReSeTnUn0g1gTeUb;c=c?c@c2g3g4gUe5gsuVe6g7g8gWe9gXe!g#g$g%g[cYeZe0e1eVnWn'g(g2eVb]c^c_c`c)g*g+g,g{c3e4e5e6eXnYn-g.g7eWb|c}c~cad/g:g;g=gbd8e9e!e#eZn0n?g@g$eXbcdddedfd[g]g^g_ggd%e'e(e)e1n2n`g{g*eYbhdidjdkd|g}g~g+eah,ebhchdh-eeh.efhghxWhh/eih:ejhkhHgK(L(M(N(eVO(yWon.imwnwdsesfsgsIg/i+bUitmumvmwm,b-b.b/bobCflkmkzc!btbFtAeVi1c2c3c4c#b$b%b'b}s:iiVmcnk;ijV*d+d}f~fAc{ kb| :bubT YlBc;b=i=bSfTf! # E Uf$ Cc% vbwbVfWfxbrcDcDfscok]ftcSbjw} ' U V W }#hnXkYkd ~#in~bjnGt] Jg8dpba$PbagbgzmAm@b[b]bGbHbIbacbcBm~satkVlVXfYfZfccdcec5c6ccgoepeCmDmEcFcGcfcgchc7c8cWiZl0l1lhsis?i9clejsQbqerepkqkHcIcJcJbKbLb!c#c@ign^ dgegEmFmKc,dLcMbNbObicjcEfqb[iksK L kclcmelbXiYiFfGfMcZizWzeknAWlnmnHtIt%cM 6 JtBWb$3hLdHlefXqYqff,vZq5h6h7hZbMd-v8h9hCW#hNdIlgf3q4qhf.v5q%h'h(h0bOd/v)h*h+hPdJlif8q9qjf:v!q-h.h/h1bQd;v:h;hb @hRdKlmf(q)qnf=v*q]h^h_h2bSd?v`h{h|hTdLlof:q;qpf@v=q~haibi3bUd[vcidieiVdMlqf[q]qrf]v^qgihiii4bWd^vjikiliXdNlsf{q|qtf_v}qnioipi5bYd`vqirisiZdOlufbrcrvf{vdruiviwi6b0d|vxiyizi1dPlwfgrhrxf}virBiCiDi7b2d~vEiFiGi3dQlyflrmrzfawnrIiJiKi8b4dbwLiMiNi5dRlAfrrsrBfcwtrPiQiRi9b6ddwSiTi

1088  

1089  

1090cdef CUresult cuGraphAddKernelNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1091 return _driver._cuGraphAddKernelNode_v2(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2f G N xcOfPfQf*iRfXlcs+cOe:cTe[c2e{c7ebd$egd*egs,b-b.b/bzcubT YlBc;b=iDc} ' U V W d pb@b[b]bXfYfZfEcFcGcZl0l1lhsis?ijsHcIcJc@iKc,dLcqb[ikslbMcLd7hNd(hPd/hb Rd_hTdbiVdiiXdpiZdwi1dDi3dKi5dRi

1092  

1093  

1094cdef CUresult cuGraphKernelNodeGetParams(CUgraphNode hNode, CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1095 return _driver._cuGraphKernelNodeGetParams_v2(hNode, nodeParams) 2f ucN vcDW,b-b.b/bzcDcd @b[b]b

1096  

1097  

1098cdef CUresult cuGraphKernelNodeSetParams(CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1099 return _driver._cuGraphKernelNodeSetParams_v2(hNode, nodeParams) 

1100  

1101  

1102cdef CUresult cuGraphAddMemcpyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1103 return _driver._cuGraphAddMemcpyNode(phGraphNode, hGraph, dependencies, numDependencies, copyParams, ctx) 23 4 5 9 TbUbVbWbXbYb+btb{ kb| :b=b! # E $ Cc% GbHbIbccdcecfcgchc9cJbKbLbMbNbObK L kclcme6 Zb0b1bb 2b3b4b5b6b7b8b9b

1104  

1105  

1106cdef CUresult cuGraphMemcpyNodeGetParams(CUgraphNode hNode, CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1107 return _driver._cuGraphMemcpyNodeGetParams(hNode, nodeParams) 2{ kbGbHbIbccdcece JbKbLbMbNbObK L F c g h i kcM 6

1108  

1109  

1110cdef CUresult cuGraphMemcpyNodeSetParams(CUgraphNode hNode, const CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1111 return _driver._cuGraphMemcpyNodeSetParams(hNode, nodeParams) 2kc

1112  

1113  

1114cdef CUresult cuGraphAddMemsetNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1115 return _driver._cuGraphAddMemsetNode(phGraphNode, hGraph, dependencies, numDependencies, memsetParams, ctx) 23 4 5 9 (b)b*byc,c-c.c/c;c=c?c@c]c^c_c`c|c}c~cadcdddedfdhdidjdkdvbwbxbd ~bacbc5c6c7c8cle!c#cicjclcme6 MdOdQdb SdUdWdYd0d2d4d6d

1116  

1117  

1118cdef CUresult cuGraphMemsetNodeGetParams(CUgraphNode hNode, CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1119 return _driver._cuGraphMemsetNodeGetParams(hNode, nodeParams) 2d acbc5c6cicjclc6

1120  

1121  

1122cdef CUresult cuGraphMemsetNodeSetParams(CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1123 return _driver._cuGraphMemsetNodeSetParams(hNode, nodeParams) 

1124  

1125  

1126cdef CUresult cuGraphAddHostNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1127 return _driver._cuGraphAddHostNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2ekfkgkhkik|#BgjkkkRnSnTnUnVnWnXnYnZn0n1n2nUiobCflkmk!bAeVi1c2c3c4c#b$b%b'b| :brcDfscoktcSbjw] 8dpba$PbagbgzmAmBm~satkVlVcgoepeCmDmWiQbqerepkqkgn^ dgegEmFmEfqbXiYiFfGfZiZq5q!qb *q=q^q}qdrirnrtr

1128  

1129  

1130cdef CUresult cuGraphHostNodeGetParams(CUgraphNode hNode, CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1131 return _driver._cuGraphHostNodeGetParams(hNode, nodeParams) 2Bg8 !bAercsctcSbPboepeQb^

1132  

1133  

1134cdef CUresult cuGraphHostNodeSetParams(CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1135 return _driver._cuGraphHostNodeSetParams(hNode, nodeParams) 

1136  

1137  

1138cdef CUresult cuGraphAddChildGraphNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

1139 return _driver._cuGraphAddChildGraphNode(phGraphNode, hGraph, dependencies, numDependencies, childGraph) 22 Bgxc+c:c[c{cbdgd8 zc!bFtAeVircDcsctcSbin8dPbBmcgQb^ LdNdPdb RdTdVdXdZd1d3d5d

1140  

1141  

1142cdef CUresult cuGraphChildGraphNodeGetGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

1143 return _driver._cuGraphChildGraphNodeGetGraph(hNode, phGraph) 22 Bgxc+c:c[c{cbdgd8 zc!bFtAeVircDcsctcSbin8dPbBmcgQb^ LdNdPdb RdTdVdXdZd1d3d5d

1144  

1145  

1146cdef CUresult cuGraphAddEmptyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil: 

1147 return _driver._cuGraphAddEmptyNode(phGraphNode, hGraph, dependencies, numDependencies) 2gVhVIeJeCg3 4 5 9 +i,i-iUkVkWkKeTbPeUbUeVeWeXeYeVb3eWb8eXb%eYb+e,e-e.exW/e:eyW.idses{ } ' U V W }#hnXkYk~#injnGtJg@iEfFfGfzeknlnmnHtItJtBWefZbCWgf0bif1bb mf2bof3bqf4bsf5buf6bwf7byf8bAf9b

1148  

1149  

1150cdef CUresult cuGraphAddEventRecordNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

1151 return _driver._cuGraphAddEventRecordNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2|fLeQeZe4e9e'e}s:iiVmcnk*d+d}f~fAc{ kbBcagbg~soeqeredgegXq3q8qb (q:q[q{qbrgrlrrr

1152  

1153  

1154cdef CUresult cuGraphEventRecordNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1155 return _driver._cuGraphEventRecordNodeGetEvent(hNode, event_out) 2}f

1156  

1157  

1158cdef CUresult cuGraphEventRecordNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

1159 return _driver._cuGraphEventRecordNodeSetEvent(hNode, event) 

1160  

1161  

1162cdef CUresult cuGraphAddEventWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

1163 return _driver._cuGraphAddEventWaitNode(phGraphNode, hGraph, dependencies, numDependencies, event) 2|fMeRe0e5e!e(emcnk;ijV}f~fbgatpereegYq4q9qb )q;q]q|qcrhrmrsr

1164  

1165  

1166cdef CUresult cuGraphEventWaitNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1167 return _driver._cuGraphEventWaitNodeGetEvent(hNode, event_out) 2~f

1168  

1169  

1170cdef CUresult cuGraphEventWaitNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

1171 return _driver._cuGraphEventWaitNodeSetEvent(hNode, event) 

1172  

1173  

1174cdef CUresult cuGraphAddExternalSemaphoresSignalNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1175 return _driver._cuGraphAddExternalSemaphoresSignalNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 

1176  

1177  

1178cdef CUresult cuGraphExternalSemaphoresSignalNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1179 return _driver._cuGraphExternalSemaphoresSignalNodeGetParams(hNode, params_out) 

1180  

1181  

1182cdef CUresult cuGraphExternalSemaphoresSignalNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1183 return _driver._cuGraphExternalSemaphoresSignalNodeSetParams(hNode, nodeParams) 

1184  

1185  

1186cdef CUresult cuGraphAddExternalSemaphoresWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1187 return _driver._cuGraphAddExternalSemaphoresWaitNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 

1188  

1189  

1190cdef CUresult cuGraphExternalSemaphoresWaitNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_WAIT_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1191 return _driver._cuGraphExternalSemaphoresWaitNodeGetParams(hNode, params_out) 

1192  

1193  

1194cdef CUresult cuGraphExternalSemaphoresWaitNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1195 return _driver._cuGraphExternalSemaphoresWaitNodeSetParams(hNode, nodeParams) 

1196  

1197  

1198cdef CUresult cuGraphAddBatchMemOpNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1199 return _driver._cuGraphAddBatchMemOpNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 

1200  

1201  

1202cdef CUresult cuGraphBatchMemOpNodeGetParams(CUgraphNode hNode, CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1203 return _driver._cuGraphBatchMemOpNodeGetParams(hNode, nodeParams_out) 

1204  

1205  

1206cdef CUresult cuGraphBatchMemOpNodeSetParams(CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1207 return _driver._cuGraphBatchMemOpNodeSetParams(hNode, nodeParams) 

1208  

1209  

1210cdef CUresult cuGraphExecBatchMemOpNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1211 return _driver._cuGraphExecBatchMemOpNodeSetParams(hGraphExec, hNode, nodeParams) 

1212  

1213  

1214cdef CUresult cuGraphAddMemAllocNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUDA_MEM_ALLOC_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1215 return _driver._cuGraphAddMemAllocNode(phGraphNode, hGraph, dependencies, numDependencies, nodeParams) 2{r|r(iFgGgVl}rWlOgIePgJeQgRg)i'd(d)dNf3 4 5 9 (b)b*byc~rasbs+i,i-iSgTgKeLeMeNeOeTb,c-c.c/cYgZgPeQeReSeTeUb;c=c?c@c4gUe5gVe6g7g8gWe9gXe!g#g$g%gYeZe0e1e2eVb]c^c_c`c+g,g3e4e5e6e7eWb|c}c~cad;g=g8e9e!e#e$eXbcdddedfd^g_g%e'e(e)e*eYbhdidjdkd~g+eah,ebhchdh-eeh.efhghhh/eih:ejhkh.ifs/i:i;i*d+dAc{ ] %c3hefffZbMd#hgfhf0bOd+hifjf1bQdb @hmfnf2bSd|hofpf3bUdeiqfrf4bWdlisftf5bYdsiufvf6b0dziwfxf7b2dGiyfzf8b4dNiAfBf9b6d

1216  

1217  

1218cdef CUresult cuGraphMemAllocNodeGetParams(CUgraphNode hNode, CUDA_MEM_ALLOC_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1219 return _driver._cuGraphMemAllocNodeGetParams(hNode, params_out) 2EWFWGWHWIWJWKWLWMWNWOWPWQWRWSWTWUWVWWWXWYWZW0WKtLtMtNtOtPtQtRtStTtUt*d+d

1220  

1221  

1222cdef CUresult cuGraphAddMemFreeNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil: 

1223 return _driver._cuGraphAddMemFreeNode(phGraphNode, hGraph, dependencies, numDependencies, dptr) 2(i)i'd(d)dNf3 4 5 9 (b)b*bycNeSe1e6e#e)eonAc%cffhfjfb nfpfrftfvfxfzfBf

1224  

1225  

1226cdef CUresult cuGraphMemFreeNodeGetParams(CUgraphNode hNode, CUdeviceptr* dptr_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1227 return _driver._cuGraphMemFreeNodeGetParams(hNode, dptr_out) 2Ac

1228  

1229  

1230cdef CUresult cuDeviceGraphMemTrim(CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil: 

1231 return _driver._cuDeviceGraphMemTrim(device) 2ocpcqc

1232  

1233  

1234cdef CUresult cuDeviceGetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

1235 return _driver._cuDeviceGetGraphMemAttribute(device, attr, value) 2ocpcqcP(%c

1236  

1237  

1238cdef CUresult cuDeviceSetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

1239 return _driver._cuDeviceSetGraphMemAttribute(device, attr, value) 2ocpcqc

1240  

1241  

1242cdef CUresult cuGraphClone(CUgraph* phGraphClone, CUgraph originalGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

1243 return _driver._cuGraphClone(phGraphClone, originalGraph) 2obmcT ;bE

1244  

1245  

1246cdef CUresult cuGraphNodeFindInClone(CUgraphNode* phNode, CUgraphNode hOriginalNode, CUgraph hClonedGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

1247 return _driver._cuGraphNodeFindInClone(phNode, hOriginalNode, hClonedGraph) 

1248  

1249  

1250cdef CUresult cuGraphNodeGetType(CUgraphNode hNode, CUgraphNodeType* type) except ?CUDA_ERROR_NOT_FOUND nogil: 

1251 return _driver._cuGraphNodeGetType(hNode, type) 2f ucN vcBgDWEWFWGWHWIWJWKWLWMWNWOWPWQWRWSWTWUWVWWWXWYWZW0WKtLtMtNtOtPtQt1WRtStTtUtQ(R(S(T(U(V(W(X(Y(Z(0(1(2(3(4(5(6(7(8(,b-b.b/b8 zc!bAe1c2c3c4c#b$b%b'b*d+d}f~fAc{ kbrcDcsc]ftcSbd Pboepee Qb^ F c g h i

1252  

1253  

1254cdef CUresult cuGraphGetNodes(CUgraph hGraph, CUgraphNode* nodes, size_t* numNodes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1255 return _driver._cuGraphGetNodes(hGraph, nodes, numNodes) 2f G ucN vcsmBgCgWkDWEWFW9(GWHWIW!(#($(JWKWLWMWNWOW%('((()(*(+(,(-(.(PWQW/(RWSWTWUW:(;(=(?(VWWWXWYWZW0W@([(](^(_(`({(|(yWtmumvmwm,b-b.b/b8 zc!bAe1c2c3c4c#b$b%b'brcDcsc]ftcSb} ' U V W d ~b] PbcgoepeCmDmEcFcGcfcgchc7c8ce Qb^ F c g h i

1256  

1257  

1258cdef CUresult cuGraphGetRootNodes(CUgraph hGraph, CUgraphNode* rootNodes, size_t* numRootNodes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1259 return _driver._cuGraphGetRootNodes(hGraph, rootNodes, numRootNodes) 

1260  

1261  

1262cdef CUresult cuGraphGetEdges(CUgraph hGraph, CUgraphNode* from_, CUgraphNode* to, CUgraphEdgeData* edgeData, size_t* numEdges) except ?CUDA_ERROR_NOT_FOUND nogil: 

1263 return _driver._cuGraphGetEdges_v2(hGraph, from_, to, edgeData, numEdges) 2` }(~(a)b)c)d)e)CgUkVkWk} ' U V W d ~b] kn

1264  

1265  

1266cdef CUresult cuGraphNodeGetDependencies(CUgraphNode hNode, CUgraphNode* dependencies, CUgraphEdgeData* edgeData, size_t* numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil: 

1267 return _driver._cuGraphNodeGetDependencies_v2(hNode, dependencies, edgeData, numDependencies) 2(i)iCg+i,i-iUkXlKtLtf)MtNtOtPtg)h)i)j)Qt1WRtStTtUtk)l)m)n)o)p)q)r).i*d+d}f~fAc{ kbBcV XkYkd knmn

1268  

1269  

1270cdef CUresult cuGraphNodeGetDependentNodes(CUgraphNode hNode, CUgraphNode* dependentNodes, CUgraphEdgeData* edgeData, size_t* numDependentNodes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1271 return _driver._cuGraphNodeGetDependentNodes_v2(hNode, dependentNodes, edgeData, numDependentNodes) 2CgVkWkKtLtMtNtOtPtQt1WRtStTtUts)t)u)v)w)x)U W hnXkYkd jnGtJgmn

1272  

1273  

1274cdef CUresult cuGraphAddDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil: 

1275 return _driver._cuGraphAddDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 2CgUkVkWkU V W hnXkYkd jnGtJg

1276  

1277  

1278cdef CUresult cuGraphRemoveDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil: 

1279 return _driver._cuGraphRemoveDependencies_v2(hGraph, from_, to, edgeData, numDependencies) 2UkVkW hnXkYkd

1280  

1281  

1282cdef CUresult cuGraphDestroyNode(CUgraphNode hNode) except ?CUDA_ERROR_NOT_FOUND nogil: 

1283 return _driver._cuGraphDestroyNode(hNode) 2xW8 obCf!btbFtAeVi1c2c3c4c#b$b%b'brcDfsctc' U V in~bjn] cgoepeCmDmEcFcGcfcgchc7c8cZl0l1l@i6 BWCW

1284  

1285  

1286cdef CUresult cuGraphInstantiate(CUgraphExec* phGraphExec, CUgraph hGraph, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1287 return _driver._cuGraphInstantiateWithFlags(phGraphExec, hGraph, flags) 2obmcT ;bE ze%cncM Jt

1288  

1289  

1290cdef CUresult cuGraphInstantiateWithParams(CUgraphExec* phGraphExec, CUgraph hGraph, CUDA_GRAPH_INSTANTIATE_PARAMS* instantiateParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1291 return _driver._cuGraphInstantiateWithParams(phGraphExec, hGraph, instantiateParams) 

1292  

1293  

1294cdef CUresult cuGraphExecGetFlags(CUgraphExec hGraphExec, cuuint64_t* flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1295 return _driver._cuGraphExecGetFlags(hGraphExec, flags) 

1296  

1297  

1298cdef CUresult cuGraphExecKernelNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1299 return _driver._cuGraphExecKernelNodeSetParams_v2(hGraphExec, hNode, nodeParams) 

1300  

1301  

1302cdef CUresult cuGraphExecMemcpyNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1303 return _driver._cuGraphExecMemcpyNodeSetParams(hGraphExec, hNode, copyParams, ctx) 

1304  

1305  

1306cdef CUresult cuGraphExecMemsetNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1307 return _driver._cuGraphExecMemsetNodeSetParams(hGraphExec, hNode, memsetParams, ctx) 

1308  

1309  

1310cdef CUresult cuGraphExecHostNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1311 return _driver._cuGraphExecHostNodeSetParams(hGraphExec, hNode, nodeParams) 

1312  

1313  

1314cdef CUresult cuGraphExecChildGraphNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

1315 return _driver._cuGraphExecChildGraphNodeSetParams(hGraphExec, hNode, childGraph) 

1316  

1317  

1318cdef CUresult cuGraphExecEventRecordNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

1319 return _driver._cuGraphExecEventRecordNodeSetEvent(hGraphExec, hNode, event) 

1320  

1321  

1322cdef CUresult cuGraphExecEventWaitNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil: 

1323 return _driver._cuGraphExecEventWaitNodeSetEvent(hGraphExec, hNode, event) 

1324  

1325  

1326cdef CUresult cuGraphExecExternalSemaphoresSignalNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1327 return _driver._cuGraphExecExternalSemaphoresSignalNodeSetParams(hGraphExec, hNode, nodeParams) 

1328  

1329  

1330cdef CUresult cuGraphExecExternalSemaphoresWaitNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1331 return _driver._cuGraphExecExternalSemaphoresWaitNodeSetParams(hGraphExec, hNode, nodeParams) 

1332  

1333  

1334cdef CUresult cuGraphNodeSetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil: 

1335 return _driver._cuGraphNodeSetEnabled(hGraphExec, hNode, isEnabled) 2?i9cle

1336  

1337  

1338cdef CUresult cuGraphNodeGetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int* isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil: 

1339 return _driver._cuGraphNodeGetEnabled(hGraphExec, hNode, isEnabled) 2?i9cle

1340  

1341  

1342cdef CUresult cuGraphUpload(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1343 return _driver._cuGraphUpload(hGraphExec, hStream) 2rbwcekfkgkhkik'd(d)dxc|fjkkkOfPfQfRf3 4 5 (b)b*blkmkokH I J X Y Z ( ) * ygzgAgocpcqc

1344  

1345  

1346cdef CUresult cuGraphLaunch(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1347 return _driver._cuGraphLaunch(hGraphExec, hStream) 27d^f_f`f{f2 f G N rbsbwc` j k l m n o p q r s t u v w x y O z A B C D P Q R S ekfkgkhkik'd(d)dNfxc|fjkkkOfPfQf*iRf3 4 5 9 (b)b*byc/iUiobCflkmkmcnk| :bubT Bc;b=i! # E $ Cc% vbwbxbDfok} ' U V W d ] H I J X Y Z ( ) * ygzgAgocpcqc8dpbPbagbgzmAm@b[b]bGbHbIbacbcWie QbqerepkqkHcIcJcJbKbLb!c#cgn^ dgegEmFmKc,dLcMbNbObicjcEfqbK L F c g h i lbXiYiFfGf0 zbMcZiye%cncM jb

1348  

1349  

1350cdef CUresult cuGraphExecDestroy(CUgraphExec hGraphExec) except ?CUDA_ERROR_NOT_FOUND nogil: 

1351 return _driver._cuGraphExecDestroy(hGraphExec) 2obmcT ;bE zencM Jt

1352  

1353  

1354cdef CUresult cuGraphDestroy(CUgraph hGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

1355 return _driver._cuGraphDestroy(hGraph) 2obmcT ;bE zeknAWlnmnHtIt%cncM b$

1356  

1357  

1358cdef CUresult cuGraphExecUpdate(CUgraphExec hGraphExec, CUgraph hGraph, CUgraphExecUpdateResultInfo* resultInfo) except ?CUDA_ERROR_NOT_FOUND nogil: 

1359 return _driver._cuGraphExecUpdate_v2(hGraphExec, hGraph, resultInfo) 

1360  

1361  

1362cdef CUresult cuGraphKernelNodeCopyAttributes(CUgraphNode dst, CUgraphNode src) except ?CUDA_ERROR_NOT_FOUND nogil: 

1363 return _driver._cuGraphKernelNodeCopyAttributes(dst, src) 

1364  

1365  

1366cdef CUresult cuGraphKernelNodeGetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, CUkernelNodeAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1367 return _driver._cuGraphKernelNodeGetAttribute(hNode, attr, value_out) 2@b[b]bKcLc[i

1368  

1369  

1370cdef CUresult cuGraphKernelNodeSetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, const CUkernelNodeAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil: 

1371 return _driver._cuGraphKernelNodeSetAttribute(hNode, attr, value) 2[i

1372  

1373  

1374cdef CUresult cuGraphDebugDotPrint(CUgraph hGraph, const char* path, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1375 return _driver._cuGraphDebugDotPrint(hGraph, path, flags) 2xmVlWl+

1376  

1377  

1378cdef CUresult cuUserObjectCreate(CUuserObject* object_out, void* ptr, CUhostFn destroy, unsigned int initialRefcount, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1379 return _driver._cuUserObjectCreate(object_out, ptr, destroy, initialRefcount, flags) 

1380  

1381  

1382cdef CUresult cuUserObjectRetain(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil: 

1383 return _driver._cuUserObjectRetain(object, count) 

1384  

1385  

1386cdef CUresult cuUserObjectRelease(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil: 

1387 return _driver._cuUserObjectRelease(object, count) 

1388  

1389  

1390cdef CUresult cuGraphRetainUserObject(CUgraph graph, CUuserObject object, unsigned int count, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1391 return _driver._cuGraphRetainUserObject(graph, object, count, flags) 

1392  

1393  

1394cdef CUresult cuGraphReleaseUserObject(CUgraph graph, CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil: 

1395 return _driver._cuGraphReleaseUserObject(graph, object, count) 

1396  

1397  

1398cdef CUresult cuGraphAddNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1399 return _driver._cuGraphAddNode_v2(phGraphNode, hGraph, dependencies, dependencyData, numDependencies, nodeParams) 2f neG j k l m n o p q r s t u v w x y O z A B C D P Q R S smUgVgWgXg0g1g2g3g'g(g)g*g-g.g/g:g?g@g[g]g`g{g|g}gHgIgtmumvmwm,b-b.b/b1c2c3c4c#b$b%b'b]f0 + zWlnM 5h6h8h9h%h'h)h*h-h.h:h;hb ]h^h`h{h~haicidigihijikinioiqiriuivixiyiBiCiEiFiIiJiLiMiPiQiSiTi

1400  

1401  

1402cdef CUresult cuGraphNodeSetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1403 return _driver._cuGraphNodeSetParams(hNode, nodeParams) 2!bSbPbM

1404  

1405  

1406cdef CUresult cuGraphExecNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1407 return _driver._cuGraphExecNodeSetParams(hGraphExec, hNode, nodeParams) 28dpbWie QbqerepkqkHcIcJcJbKbLb!c#cgnEfqbF c lbXiYiM

1408  

1409  

1410cdef CUresult cuGraphConditionalHandleCreate(CUgraphConditionalHandle* pHandle_out, CUgraph hGraph, CUcontext ctx, unsigned int defaultLaunchValue, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1411 return _driver._cuGraphConditionalHandleCreate(pHandle_out, hGraph, ctx, defaultLaunchValue, flags) 2f neG ymj k l m n o p q r s t u v w x y O z A B C D P Q R S smUgVgWgXg0g1g2g3g'g(g)g*g-g.g/g:g?g@g[g]g`g{g|g}gHgeVIgtmumvmwm,b-b.b/b1c2c3c4c#b$b%b'b]f0 + zWHl5h6h8h9hIl%h'h)h*hJl-h.h:h;hb Kl]h^h`h{hLl~haicidiMlgihijikiNlnioiqiriOluivixiyiPlBiCiEiFiQlIiJiLiMiRlPiQiSiTi

1412  

1413  

1414cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize) except ?CUDA_ERROR_NOT_FOUND nogil: 

1415 return _driver._cuOccupancyMaxActiveBlocksPerMultiprocessor(numBlocks, func, blockSize, dynamicSMemSize) 2KdQsRsSsTsUsVsWsXsYsZs0s1s2s3s4s5s6s7s

1416  

1417  

1418cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1419 return _driver._cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(numBlocks, func, blockSize, dynamicSMemSize, flags) 

1420  

1421  

1422cdef CUresult cuOccupancyMaxPotentialBlockSize(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit) except ?CUDA_ERROR_NOT_FOUND nogil: 

1423 return _driver._cuOccupancyMaxPotentialBlockSize(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit) 2)x*x+x,x-x.x/x:x;x=x?x@x[x]x^x_x`x{x|x}x~x

1424  

1425  

1426cdef CUresult cuOccupancyMaxPotentialBlockSizeWithFlags(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1427 return _driver._cuOccupancyMaxPotentialBlockSizeWithFlags(minGridSize, blockSize, func, blockSizeToDynamicSMemSize, dynamicSMemSize, blockSizeLimit, flags) 

1428  

1429  

1430cdef CUresult cuOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, CUfunction func, int numBlocks, int blockSize) except ?CUDA_ERROR_NOT_FOUND nogil: 

1431 return _driver._cuOccupancyAvailableDynamicSMemPerBlock(dynamicSmemSize, func, numBlocks, blockSize) 2!x#x$x%x'x(x

1432  

1433  

1434cdef CUresult cuOccupancyMaxPotentialClusterSize(int* clusterSize, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil: 

1435 return _driver._cuOccupancyMaxPotentialClusterSize(clusterSize, func, config) 

1436  

1437  

1438cdef CUresult cuOccupancyMaxActiveClusters(int* numClusters, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil: 

1439 return _driver._cuOccupancyMaxActiveClusters(numClusters, func, config) 

1440  

1441  

1442cdef CUresult cuTexRefSetArray(CUtexref hTexRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1443 return _driver._cuTexRefSetArray(hTexRef, hArray, Flags) 

1444  

1445  

1446cdef CUresult cuTexRefSetMipmappedArray(CUtexref hTexRef, CUmipmappedArray hMipmappedArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1447 return _driver._cuTexRefSetMipmappedArray(hTexRef, hMipmappedArray, Flags) 

1448  

1449  

1450cdef CUresult cuTexRefSetAddress(size_t* ByteOffset, CUtexref hTexRef, CUdeviceptr dptr, size_t bytes) except ?CUDA_ERROR_NOT_FOUND nogil: 

1451 return _driver._cuTexRefSetAddress_v2(ByteOffset, hTexRef, dptr, bytes) 

1452  

1453  

1454cdef CUresult cuTexRefSetAddress2D(CUtexref hTexRef, const CUDA_ARRAY_DESCRIPTOR* desc, CUdeviceptr dptr, size_t Pitch) except ?CUDA_ERROR_NOT_FOUND nogil: 

1455 return _driver._cuTexRefSetAddress2D_v3(hTexRef, desc, dptr, Pitch) 

1456  

1457  

1458cdef CUresult cuTexRefSetFormat(CUtexref hTexRef, CUarray_format fmt, int NumPackedComponents) except ?CUDA_ERROR_NOT_FOUND nogil: 

1459 return _driver._cuTexRefSetFormat(hTexRef, fmt, NumPackedComponents) 

1460  

1461  

1462cdef CUresult cuTexRefSetAddressMode(CUtexref hTexRef, int dim, CUaddress_mode am) except ?CUDA_ERROR_NOT_FOUND nogil: 

1463 return _driver._cuTexRefSetAddressMode(hTexRef, dim, am) 

1464  

1465  

1466cdef CUresult cuTexRefSetFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil: 

1467 return _driver._cuTexRefSetFilterMode(hTexRef, fm) 

1468  

1469  

1470cdef CUresult cuTexRefSetMipmapFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil: 

1471 return _driver._cuTexRefSetMipmapFilterMode(hTexRef, fm) 

1472  

1473  

1474cdef CUresult cuTexRefSetMipmapLevelBias(CUtexref hTexRef, float bias) except ?CUDA_ERROR_NOT_FOUND nogil: 

1475 return _driver._cuTexRefSetMipmapLevelBias(hTexRef, bias) 

1476  

1477  

1478cdef CUresult cuTexRefSetMipmapLevelClamp(CUtexref hTexRef, float minMipmapLevelClamp, float maxMipmapLevelClamp) except ?CUDA_ERROR_NOT_FOUND nogil: 

1479 return _driver._cuTexRefSetMipmapLevelClamp(hTexRef, minMipmapLevelClamp, maxMipmapLevelClamp) 

1480  

1481  

1482cdef CUresult cuTexRefSetMaxAnisotropy(CUtexref hTexRef, unsigned int maxAniso) except ?CUDA_ERROR_NOT_FOUND nogil: 

1483 return _driver._cuTexRefSetMaxAnisotropy(hTexRef, maxAniso) 

1484  

1485  

1486cdef CUresult cuTexRefSetBorderColor(CUtexref hTexRef, float* pBorderColor) except ?CUDA_ERROR_NOT_FOUND nogil: 

1487 return _driver._cuTexRefSetBorderColor(hTexRef, pBorderColor) 

1488  

1489  

1490cdef CUresult cuTexRefSetFlags(CUtexref hTexRef, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1491 return _driver._cuTexRefSetFlags(hTexRef, Flags) 

1492  

1493  

1494cdef CUresult cuTexRefGetAddress(CUdeviceptr* pdptr, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1495 return _driver._cuTexRefGetAddress_v2(pdptr, hTexRef) 

1496  

1497  

1498cdef CUresult cuTexRefGetArray(CUarray* phArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1499 return _driver._cuTexRefGetArray(phArray, hTexRef) 

1500  

1501  

1502cdef CUresult cuTexRefGetMipmappedArray(CUmipmappedArray* phMipmappedArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1503 return _driver._cuTexRefGetMipmappedArray(phMipmappedArray, hTexRef) 

1504  

1505  

1506cdef CUresult cuTexRefGetAddressMode(CUaddress_mode* pam, CUtexref hTexRef, int dim) except ?CUDA_ERROR_NOT_FOUND nogil: 

1507 return _driver._cuTexRefGetAddressMode(pam, hTexRef, dim) 

1508  

1509  

1510cdef CUresult cuTexRefGetFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1511 return _driver._cuTexRefGetFilterMode(pfm, hTexRef) 

1512  

1513  

1514cdef CUresult cuTexRefGetFormat(CUarray_format* pFormat, int* pNumChannels, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1515 return _driver._cuTexRefGetFormat(pFormat, pNumChannels, hTexRef) 

1516  

1517  

1518cdef CUresult cuTexRefGetMipmapFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1519 return _driver._cuTexRefGetMipmapFilterMode(pfm, hTexRef) 

1520  

1521  

1522cdef CUresult cuTexRefGetMipmapLevelBias(float* pbias, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1523 return _driver._cuTexRefGetMipmapLevelBias(pbias, hTexRef) 

1524  

1525  

1526cdef CUresult cuTexRefGetMipmapLevelClamp(float* pminMipmapLevelClamp, float* pmaxMipmapLevelClamp, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1527 return _driver._cuTexRefGetMipmapLevelClamp(pminMipmapLevelClamp, pmaxMipmapLevelClamp, hTexRef) 

1528  

1529  

1530cdef CUresult cuTexRefGetMaxAnisotropy(int* pmaxAniso, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1531 return _driver._cuTexRefGetMaxAnisotropy(pmaxAniso, hTexRef) 

1532  

1533  

1534cdef CUresult cuTexRefGetBorderColor(float* pBorderColor, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1535 return _driver._cuTexRefGetBorderColor(pBorderColor, hTexRef) 

1536  

1537  

1538cdef CUresult cuTexRefGetFlags(unsigned int* pFlags, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1539 return _driver._cuTexRefGetFlags(pFlags, hTexRef) 

1540  

1541  

1542cdef CUresult cuTexRefCreate(CUtexref* pTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1543 return _driver._cuTexRefCreate(pTexRef) 

1544  

1545  

1546cdef CUresult cuTexRefDestroy(CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1547 return _driver._cuTexRefDestroy(hTexRef) 

1548  

1549  

1550cdef CUresult cuSurfRefSetArray(CUsurfref hSurfRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1551 return _driver._cuSurfRefSetArray(hSurfRef, hArray, Flags) 

1552  

1553  

1554cdef CUresult cuSurfRefGetArray(CUarray* phArray, CUsurfref hSurfRef) except ?CUDA_ERROR_NOT_FOUND nogil: 

1555 return _driver._cuSurfRefGetArray(phArray, hSurfRef) 

1556  

1557  

1558cdef CUresult cuTexObjectCreate(CUtexObject* pTexObject, const CUDA_RESOURCE_DESC* pResDesc, const CUDA_TEXTURE_DESC* pTexDesc, const CUDA_RESOURCE_VIEW_DESC* pResViewDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

1559 return _driver._cuTexObjectCreate(pTexObject, pResDesc, pTexDesc, pResViewDesc) 

1560  

1561  

1562cdef CUresult cuTexObjectDestroy(CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1563 return _driver._cuTexObjectDestroy(texObject) 

1564  

1565  

1566cdef CUresult cuTexObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1567 return _driver._cuTexObjectGetResourceDesc(pResDesc, texObject) 

1568  

1569  

1570cdef CUresult cuTexObjectGetTextureDesc(CUDA_TEXTURE_DESC* pTexDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1571 return _driver._cuTexObjectGetTextureDesc(pTexDesc, texObject) 

1572  

1573  

1574cdef CUresult cuTexObjectGetResourceViewDesc(CUDA_RESOURCE_VIEW_DESC* pResViewDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1575 return _driver._cuTexObjectGetResourceViewDesc(pResViewDesc, texObject) 

1576  

1577  

1578cdef CUresult cuSurfObjectCreate(CUsurfObject* pSurfObject, const CUDA_RESOURCE_DESC* pResDesc) except ?CUDA_ERROR_NOT_FOUND nogil: 

1579 return _driver._cuSurfObjectCreate(pSurfObject, pResDesc) 

1580  

1581  

1582cdef CUresult cuSurfObjectDestroy(CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1583 return _driver._cuSurfObjectDestroy(surfObject) 

1584  

1585  

1586cdef CUresult cuSurfObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil: 

1587 return _driver._cuSurfObjectGetResourceDesc(pResDesc, surfObject) 

1588  

1589  

1590cdef CUresult cuTensorMapEncodeTiled(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, const cuuint32_t* boxDim, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil: 

1591 return _driver._cuTensorMapEncodeTiled(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, boxDim, elementStrides, interleave, swizzle, l2Promotion, oobFill) 

1592  

1593  

1594cdef CUresult cuTensorMapEncodeIm2col(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, const int* pixelBoxLowerCorner, const int* pixelBoxUpperCorner, cuuint32_t channelsPerPixel, cuuint32_t pixelsPerColumn, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil: 

1595 return _driver._cuTensorMapEncodeIm2col(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCorner, pixelBoxUpperCorner, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, swizzle, l2Promotion, oobFill) 

1596  

1597  

1598cdef CUresult cuTensorMapEncodeIm2colWide(CUtensorMap* tensorMap, CUtensorMapDataType tensorDataType, cuuint32_t tensorRank, void* globalAddress, const cuuint64_t* globalDim, const cuuint64_t* globalStrides, int pixelBoxLowerCornerWidth, int pixelBoxUpperCornerWidth, cuuint32_t channelsPerPixel, cuuint32_t pixelsPerColumn, const cuuint32_t* elementStrides, CUtensorMapInterleave interleave, CUtensorMapIm2ColWideMode mode, CUtensorMapSwizzle swizzle, CUtensorMapL2promotion l2Promotion, CUtensorMapFloatOOBfill oobFill) except ?CUDA_ERROR_NOT_FOUND nogil: 

1599 return _driver._cuTensorMapEncodeIm2colWide(tensorMap, tensorDataType, tensorRank, globalAddress, globalDim, globalStrides, pixelBoxLowerCornerWidth, pixelBoxUpperCornerWidth, channelsPerPixel, pixelsPerColumn, elementStrides, interleave, mode, swizzle, l2Promotion, oobFill) 

1600  

1601  

1602cdef CUresult cuTensorMapReplaceAddress(CUtensorMap* tensorMap, void* globalAddress) except ?CUDA_ERROR_NOT_FOUND nogil: 

1603 return _driver._cuTensorMapReplaceAddress(tensorMap, globalAddress) 

1604  

1605  

1606cdef CUresult cuDeviceCanAccessPeer(int* canAccessPeer, CUdevice dev, CUdevice peerDev) except ?CUDA_ERROR_NOT_FOUND nogil: 

1607 return _driver._cuDeviceCanAccessPeer(canAccessPeer, dev, peerDev) 

1608  

1609  

1610cdef CUresult cuCtxEnablePeerAccess(CUcontext peerContext, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1611 return _driver._cuCtxEnablePeerAccess(peerContext, Flags) 

1612  

1613  

1614cdef CUresult cuCtxDisablePeerAccess(CUcontext peerContext) except ?CUDA_ERROR_NOT_FOUND nogil: 

1615 return _driver._cuCtxDisablePeerAccess(peerContext) 

1616  

1617  

1618cdef CUresult cuDeviceGetP2PAttribute(int* value, CUdevice_P2PAttribute attrib, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil: 

1619 return _driver._cuDeviceGetP2PAttribute(value, attrib, srcDevice, dstDevice) 

1620  

1621  

1622cdef CUresult cuGraphicsUnregisterResource(CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil: 

1623 return _driver._cuGraphicsUnregisterResource(resource) 

1624  

1625  

1626cdef CUresult cuGraphicsSubResourceGetMappedArray(CUarray* pArray, CUgraphicsResource resource, unsigned int arrayIndex, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil: 

1627 return _driver._cuGraphicsSubResourceGetMappedArray(pArray, resource, arrayIndex, mipLevel) 

1628  

1629  

1630cdef CUresult cuGraphicsResourceGetMappedMipmappedArray(CUmipmappedArray* pMipmappedArray, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil: 

1631 return _driver._cuGraphicsResourceGetMappedMipmappedArray(pMipmappedArray, resource) 

1632  

1633  

1634cdef CUresult cuGraphicsResourceGetMappedPointer(CUdeviceptr* pDevPtr, size_t* pSize, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil: 

1635 return _driver._cuGraphicsResourceGetMappedPointer_v2(pDevPtr, pSize, resource) 2ctdtetftgthtGmitjtktHm

1636  

1637  

1638cdef CUresult cuGraphicsResourceSetMapFlags(CUgraphicsResource resource, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1639 return _driver._cuGraphicsResourceSetMapFlags_v2(resource, flags) 

1640  

1641  

1642cdef CUresult cuGraphicsMapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1643 return _driver._cuGraphicsMapResources(count, resources, hStream) 2ctdtetftgthtGmitjtktHm

1644  

1645  

1646cdef CUresult cuGraphicsUnmapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1647 return _driver._cuGraphicsUnmapResources(count, resources, hStream) 

1648  

1649  

1650cdef CUresult cuGetProcAddress(const char* symbol, void** pfn, int cudaVersion, cuuint64_t flags, CUdriverProcAddressQueryResult* symbolStatus) except ?CUDA_ERROR_NOT_FOUND nogil: 

1651 return _driver._cuGetProcAddress_v2(symbol, pfn, cudaVersion, flags, symbolStatus) 

1652  

1653  

1654cdef CUresult cuCoredumpGetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil: 

1655 return _driver._cuCoredumpGetAttribute(attrib, value, size) 

1656  

1657  

1658cdef CUresult cuCoredumpGetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil: 

1659 return _driver._cuCoredumpGetAttributeGlobal(attrib, value, size) 2c$

1660  

1661  

1662cdef CUresult cuCoredumpSetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil: 

1663 return _driver._cuCoredumpSetAttribute(attrib, value, size) 

1664  

1665  

1666cdef CUresult cuCoredumpSetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil: 

1667 return _driver._cuCoredumpSetAttributeGlobal(attrib, value, size) 2c$

1668  

1669  

1670cdef CUresult cuGetExportTable(const void** ppExportTable, const CUuuid* pExportTableId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1671 return _driver._cuGetExportTable(ppExportTable, pExportTableId) 

1672  

1673  

1674cdef CUresult cuGreenCtxCreate(CUgreenCtx* phCtx, CUdevResourceDesc desc, CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1675 return _driver._cuGreenCtxCreate(phCtx, desc, dev, flags) 

1676  

1677  

1678cdef CUresult cuGreenCtxDestroy(CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1679 return _driver._cuGreenCtxDestroy(hCtx) 

1680  

1681  

1682cdef CUresult cuCtxFromGreenCtx(CUcontext* pContext, CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1683 return _driver._cuCtxFromGreenCtx(pContext, hCtx) 

1684  

1685  

1686cdef CUresult cuDeviceGetDevResource(CUdevice device, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil: 

1687 return _driver._cuDeviceGetDevResource(device, resource, type) 2d$e$Bv)oCvDv*oAl+o,o-o.o/o:o;o=o?o@oEvFvGvHvIvJvKvLvMvNvOvPvQvRvSvTvUvVvWvXvYvZv0v1v2v3v[o4v

1688  

1689  

1690cdef CUresult cuCtxGetDevResource(CUcontext hCtx, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil: 

1691 return _driver._cuCtxGetDevResource(hCtx, resource, type) 2y)z)

1692  

1693  

1694cdef CUresult cuGreenCtxGetDevResource(CUgreenCtx hCtx, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil: 

1695 return _driver._cuGreenCtxGetDevResource(hCtx, resource, type) 2fVA)B)

1696  

1697  

1698cdef CUresult cuDevSmResourceSplitByCount(CUdevResource* result, unsigned int* nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, unsigned int minCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

1699 return _driver._cuDevSmResourceSplitByCount(result, nbGroups, input, remainder, flags, minCount) 2e$

1700  

1701  

1702cdef CUresult cuDevResourceGenerateDesc(CUdevResourceDesc* phDesc, CUdevResource* resources, unsigned int nbResources) except ?CUDA_ERROR_NOT_FOUND nogil: 

1703 return _driver._cuDevResourceGenerateDesc(phDesc, resources, nbResources) 

1704  

1705  

1706cdef CUresult cuGreenCtxRecordEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

1707 return _driver._cuGreenCtxRecordEvent(hCtx, hEvent) 

1708  

1709  

1710cdef CUresult cuGreenCtxWaitEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil: 

1711 return _driver._cuGreenCtxWaitEvent(hCtx, hEvent) 

1712  

1713  

1714cdef CUresult cuStreamGetGreenCtx(CUstream hStream, CUgreenCtx* phCtx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1715 return _driver._cuStreamGetGreenCtx(hStream, phCtx) 

1716  

1717  

1718cdef CUresult cuGreenCtxStreamCreate(CUstream* phStream, CUgreenCtx greenCtx, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil: 

1719 return _driver._cuGreenCtxStreamCreate(phStream, greenCtx, flags, priority) 

1720  

1721  

1722cdef CUresult cuLogsRegisterCallback(CUlogsCallback callbackFunc, void* userData, CUlogsCallbackHandle* callback_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

1723 return _driver._cuLogsRegisterCallback(callbackFunc, userData, callback_out) 2nn

1724  

1725  

1726cdef CUresult cuLogsUnregisterCallback(CUlogsCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

1727 return _driver._cuLogsUnregisterCallback(callback) 2nn

1728  

1729  

1730cdef CUresult cuLogsCurrent(CUlogIterator* iterator_out, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1731 return _driver._cuLogsCurrent(iterator_out, flags) 2nn

1732  

1733  

1734cdef CUresult cuLogsDumpToFile(CUlogIterator* iterator, const char* pathToFile, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1735 return _driver._cuLogsDumpToFile(iterator, pathToFile, flags) 2nn

1736  

1737  

1738cdef CUresult cuLogsDumpToMemory(CUlogIterator* iterator, char* buffer, size_t* size, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1739 return _driver._cuLogsDumpToMemory(iterator, buffer, size, flags) 2nn

1740  

1741  

1742cdef CUresult cuCheckpointProcessGetRestoreThreadId(int pid, int* tid) except ?CUDA_ERROR_NOT_FOUND nogil: 

1743 return _driver._cuCheckpointProcessGetRestoreThreadId(pid, tid) 

1744  

1745  

1746cdef CUresult cuCheckpointProcessGetState(int pid, CUprocessState* state) except ?CUDA_ERROR_NOT_FOUND nogil: 

1747 return _driver._cuCheckpointProcessGetState(pid, state) 2C)

1748  

1749  

1750cdef CUresult cuCheckpointProcessLock(int pid, CUcheckpointLockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil: 

1751 return _driver._cuCheckpointProcessLock(pid, args) 

1752  

1753  

1754cdef CUresult cuCheckpointProcessCheckpoint(int pid, CUcheckpointCheckpointArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil: 

1755 return _driver._cuCheckpointProcessCheckpoint(pid, args) 

1756  

1757  

1758cdef CUresult cuCheckpointProcessRestore(int pid, CUcheckpointRestoreArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil: 

1759 return _driver._cuCheckpointProcessRestore(pid, args) 

1760  

1761  

1762cdef CUresult cuCheckpointProcessUnlock(int pid, CUcheckpointUnlockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil: 

1763 return _driver._cuCheckpointProcessUnlock(pid, args) 

1764  

1765  

1766cdef CUresult cuGraphicsEGLRegisterImage(CUgraphicsResource* pCudaResource, EGLImageKHR image, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1767 return _driver._cuGraphicsEGLRegisterImage(pCudaResource, image, flags) 

1768  

1769  

1770cdef CUresult cuEGLStreamConsumerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1771 return _driver._cuEGLStreamConsumerConnect(conn, stream) 

1772  

1773  

1774cdef CUresult cuEGLStreamConsumerConnectWithFlags(CUeglStreamConnection* conn, EGLStreamKHR stream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1775 return _driver._cuEGLStreamConsumerConnectWithFlags(conn, stream, flags) 

1776  

1777  

1778cdef CUresult cuEGLStreamConsumerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil: 

1779 return _driver._cuEGLStreamConsumerDisconnect(conn) 

1780  

1781  

1782cdef CUresult cuEGLStreamConsumerAcquireFrame(CUeglStreamConnection* conn, CUgraphicsResource* pCudaResource, CUstream* pStream, unsigned int timeout) except ?CUDA_ERROR_NOT_FOUND nogil: 

1783 return _driver._cuEGLStreamConsumerAcquireFrame(conn, pCudaResource, pStream, timeout) 

1784  

1785  

1786cdef CUresult cuEGLStreamConsumerReleaseFrame(CUeglStreamConnection* conn, CUgraphicsResource pCudaResource, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1787 return _driver._cuEGLStreamConsumerReleaseFrame(conn, pCudaResource, pStream) 

1788  

1789  

1790cdef CUresult cuEGLStreamProducerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream, EGLint width, EGLint height) except ?CUDA_ERROR_NOT_FOUND nogil: 

1791 return _driver._cuEGLStreamProducerConnect(conn, stream, width, height) 

1792  

1793  

1794cdef CUresult cuEGLStreamProducerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil: 

1795 return _driver._cuEGLStreamProducerDisconnect(conn) 

1796  

1797  

1798cdef CUresult cuEGLStreamProducerPresentFrame(CUeglStreamConnection* conn, CUeglFrame eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1799 return _driver._cuEGLStreamProducerPresentFrame(conn, eglframe, pStream) 

1800  

1801  

1802cdef CUresult cuEGLStreamProducerReturnFrame(CUeglStreamConnection* conn, CUeglFrame* eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1803 return _driver._cuEGLStreamProducerReturnFrame(conn, eglframe, pStream) 

1804  

1805  

1806cdef CUresult cuGraphicsResourceGetMappedEglFrame(CUeglFrame* eglFrame, CUgraphicsResource resource, unsigned int index, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil: 

1807 return _driver._cuGraphicsResourceGetMappedEglFrame(eglFrame, resource, index, mipLevel) 

1808  

1809  

1810cdef CUresult cuEventCreateFromEGLSync(CUevent* phEvent, EGLSyncKHR eglSync, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1811 return _driver._cuEventCreateFromEGLSync(phEvent, eglSync, flags) 

1812  

1813  

1814cdef CUresult cuGraphicsGLRegisterBuffer(CUgraphicsResource* pCudaResource, GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1815 return _driver._cuGraphicsGLRegisterBuffer(pCudaResource, buffer, Flags) 2ctdt'!etftgthtGm(!)!*!+!itjt,!.!/!:!;!ktHm=!?!

1816  

1817  

1818cdef CUresult cuGraphicsGLRegisterImage(CUgraphicsResource* pCudaResource, GLuint image, GLenum target, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1819 return _driver._cuGraphicsGLRegisterImage(pCudaResource, image, target, Flags) 2-!

1820  

1821  

1822cdef CUresult cuGLGetDevices(unsigned int* pCudaDeviceCount, CUdevice* pCudaDevices, unsigned int cudaDeviceCount, CUGLDeviceList deviceList) except ?CUDA_ERROR_NOT_FOUND nogil: 

1823 return _driver._cuGLGetDevices_v2(pCudaDeviceCount, pCudaDevices, cudaDeviceCount, deviceList) 

1824  

1825  

1826cdef CUresult cuGLCtxCreate(CUcontext* pCtx, unsigned int Flags, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil: 

1827 return _driver._cuGLCtxCreate_v2(pCtx, Flags, device) 

1828  

1829  

1830cdef CUresult cuGLInit() except ?CUDA_ERROR_NOT_FOUND nogil: 

1831 return _driver._cuGLInit() 

1832  

1833  

1834cdef CUresult cuGLRegisterBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil: 

1835 return _driver._cuGLRegisterBufferObject(buffer) 

1836  

1837  

1838cdef CUresult cuGLMapBufferObject(CUdeviceptr* dptr, size_t* size, GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil: 

1839 return _driver._cuGLMapBufferObject_v2(dptr, size, buffer) 

1840  

1841  

1842cdef CUresult cuGLUnmapBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil: 

1843 return _driver._cuGLUnmapBufferObject(buffer) 

1844  

1845  

1846cdef CUresult cuGLUnregisterBufferObject(GLuint buffer) except ?CUDA_ERROR_NOT_FOUND nogil: 

1847 return _driver._cuGLUnregisterBufferObject(buffer) 

1848  

1849  

1850cdef CUresult cuGLSetBufferObjectMapFlags(GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1851 return _driver._cuGLSetBufferObjectMapFlags(buffer, Flags) 

1852  

1853  

1854cdef CUresult cuGLMapBufferObjectAsync(CUdeviceptr* dptr, size_t* size, GLuint buffer, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1855 return _driver._cuGLMapBufferObjectAsync_v2(dptr, size, buffer, hStream) 

1856  

1857  

1858cdef CUresult cuGLUnmapBufferObjectAsync(GLuint buffer, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1859 return _driver._cuGLUnmapBufferObjectAsync(buffer, hStream) 

1860  

1861  

1862cdef CUresult cuProfilerInitialize(const char* configFile, const char* outputFile, CUoutput_mode outputMode) except ?CUDA_ERROR_NOT_FOUND nogil: 

1863 return _driver._cuProfilerInitialize(configFile, outputFile, outputMode) 

1864  

1865  

1866cdef CUresult cuProfilerStart() except ?CUDA_ERROR_NOT_FOUND nogil: 

1867 return _driver._cuProfilerStart() 2f$

1868  

1869  

1870cdef CUresult cuProfilerStop() except ?CUDA_ERROR_NOT_FOUND nogil: 

1871 return _driver._cuProfilerStop() 2f$

1872  

1873  

1874cdef CUresult cuVDPAUGetDevice(CUdevice* pDevice, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil: 

1875 return _driver._cuVDPAUGetDevice(pDevice, vdpDevice, vdpGetProcAddress) 

1876  

1877  

1878cdef CUresult cuVDPAUCtxCreate(CUcontext* pCtx, unsigned int flags, CUdevice device, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil: 

1879 return _driver._cuVDPAUCtxCreate_v2(pCtx, flags, device, vdpDevice, vdpGetProcAddress) 

1880  

1881  

1882cdef CUresult cuGraphicsVDPAURegisterVideoSurface(CUgraphicsResource* pCudaResource, VdpVideoSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1883 return _driver._cuGraphicsVDPAURegisterVideoSurface(pCudaResource, vdpSurface, flags) 

1884  

1885  

1886cdef CUresult cuGraphicsVDPAURegisterOutputSurface(CUgraphicsResource* pCudaResource, VdpOutputSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1887 return _driver._cuGraphicsVDPAURegisterOutputSurface(pCudaResource, vdpSurface, flags) 

1888  

1889  

1890cdef CUresult cuDeviceGetHostAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

1891 return _driver._cuDeviceGetHostAtomicCapabilities(capabilities, operations, count, dev) 

1892  

1893  

1894cdef CUresult cuCtxGetDevice_v2(CUdevice* device, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1895 return _driver._cuCtxGetDevice_v2(device, ctx) 

1896  

1897  

1898cdef CUresult cuCtxSynchronize_v2(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil: 

1899 return _driver._cuCtxSynchronize_v2(ctx) 

1900  

1901  

1902cdef CUresult cuMemcpyBatchAsync(CUdeviceptr* dsts, CUdeviceptr* srcs, size_t* sizes, size_t count, CUmemcpyAttributes* attrs, size_t* attrsIdxs, size_t numAttrs, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1903 return _driver._cuMemcpyBatchAsync_v2(dsts, srcs, sizes, count, attrs, attrsIdxs, numAttrs, hStream) 2hgvewk~ abwe$cCbigbbvWxk, - . cbykzkAkBk

1904  

1905  

1906cdef CUresult cuMemcpy3DBatchAsync(size_t numOps, CUDA_MEMCPY3D_BATCH_OP* opList, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1907 return _driver._cuMemcpy3DBatchAsync_v2(numOps, opList, flags, hStream) 

1908  

1909  

1910cdef CUresult cuMemGetDefaultMemPool(CUmemoryPool* pool_out, CUmemLocation* location, CUmemAllocationType type) except ?CUDA_ERROR_NOT_FOUND nogil: 

1911 return _driver._cuMemGetDefaultMemPool(pool_out, location, type) 

1912  

1913  

1914cdef CUresult cuMemGetMemPool(CUmemoryPool* pool, CUmemLocation* location, CUmemAllocationType type) except ?CUDA_ERROR_NOT_FOUND nogil: 

1915 return _driver._cuMemGetMemPool(pool, location, type) 22l, - . : ; = 7k8k+kmh]esenh^eoh_eph`e/k:k;k=k?k@k[k'lpsqs(lrssstsusvsoj)lqj,lJxrjKx-lLx.lMx/lNx:lOxsjPx;lQx=lvj[lxj

1916  

1917  

1918cdef CUresult cuMemSetMemPool(CUmemLocation* location, CUmemAllocationType type, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil: 

1919 return _driver._cuMemSetMemPool(location, type, pool) 

1920  

1921  

1922cdef CUresult cuMemPrefetchBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, CUmemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1923 return _driver._cuMemPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 2fnTkdnen

1924  

1925  

1926cdef CUresult cuMemDiscardBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1927 return _driver._cuMemDiscardBatchAsync(dptrs, sizes, count, flags, hStream) 2fnwtxt

1928  

1929  

1930cdef CUresult cuMemDiscardAndPrefetchBatchAsync(CUdeviceptr* dptrs, size_t* sizes, size_t count, CUmemLocation* prefetchLocs, size_t* prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1931 return _driver._cuMemDiscardAndPrefetchBatchAsync(dptrs, sizes, count, prefetchLocs, prefetchLocIdxs, numPrefetchLocs, flags, hStream) 2Tkse

1932  

1933  

1934cdef CUresult cuDeviceGetP2PAtomicCapabilities(unsigned int* capabilities, const CUatomicOperation* operations, unsigned int count, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil: 

1935 return _driver._cuDeviceGetP2PAtomicCapabilities(capabilities, operations, count, srcDevice, dstDevice) 

1936  

1937  

1938cdef CUresult cuGreenCtxGetId(CUgreenCtx greenCtx, unsigned long long* greenCtxId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1939 return _driver._cuGreenCtxGetId(greenCtx, greenCtxId) 

1940  

1941  

1942cdef CUresult cuMulticastBindMem_v2(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, CUmemGenericAllocationHandle memHandle, size_t memOffset, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1943 return _driver._cuMulticastBindMem_v2(mcHandle, dev, mcOffset, memHandle, memOffset, size, flags) 

1944  

1945  

1946cdef CUresult cuMulticastBindAddr_v2(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

1947 return _driver._cuMulticastBindAddr_v2(mcHandle, dev, mcOffset, memptr, size, flags) 

1948  

1949  

1950cdef CUresult cuGraphNodeGetContainingGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil: 

1951 return _driver._cuGraphNodeGetContainingGraph(hNode, phGraph) 2ln

1952  

1953  

1954cdef CUresult cuGraphNodeGetLocalId(CUgraphNode hNode, unsigned int* nodeId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1955 return _driver._cuGraphNodeGetLocalId(hNode, nodeId) 2Ht

1956  

1957  

1958cdef CUresult cuGraphNodeGetToolsId(CUgraphNode hNode, unsigned long long* toolsNodeId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1959 return _driver._cuGraphNodeGetToolsId(hNode, toolsNodeId) 2It

1960  

1961  

1962cdef CUresult cuGraphGetId(CUgraph hGraph, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1963 return _driver._cuGraphGetId(hGraph, graphId) 2AW

1964  

1965  

1966cdef CUresult cuGraphExecGetId(CUgraphExec hGraphExec, unsigned int* graphId) except ?CUDA_ERROR_NOT_FOUND nogil: 

1967 return _driver._cuGraphExecGetId(hGraphExec, graphId) 2ze

1968  

1969  

1970cdef CUresult cuDevSmResourceSplit(CUdevResource* result, unsigned int nbGroups, const CUdevResource* input, CUdevResource* remainder, unsigned int flags, CU_DEV_SM_RESOURCE_GROUP_PARAMS* groupParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1971 return _driver._cuDevSmResourceSplit(result, nbGroups, input, remainder, flags, groupParams) 2d$fV)o*oAl? @ -o.o/o:o;o=o?o@oD)E)F)G)H)I)J)V![oW!

1972  

1973  

1974cdef CUresult cuStreamGetDevResource(CUstream hStream, CUdevResource* resource, CUdevResourceType type) except ?CUDA_ERROR_NOT_FOUND nogil: 

1975 return _driver._cuStreamGetDevResource(hStream, resource, type) 2sW

1976  

1977  

1978cdef CUresult cuKernelGetParamCount(CUkernel kernel, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

1979 return _driver._cuKernelGetParamCount(kernel, paramCount) 

1980  

1981  

1982cdef CUresult cuMemcpyWithAttributesAsync(CUdeviceptr dst, CUdeviceptr src, size_t size, CUmemcpyAttributes* attr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1983 return _driver._cuMemcpyWithAttributesAsync(dst, src, size, attr, hStream) 2/ jgkg: ; = lgmgngRmogpgqgrg

1984  

1985  

1986cdef CUresult cuMemcpy3DWithAttributesAsync(CUDA_MEMCPY3D_BATCH_OP* op, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1987 return _driver._cuMemcpy3DWithAttributesAsync(op, flags, hStream) 

1988  

1989  

1990cdef CUresult cuStreamBeginCaptureToCig(CUstream hStream, CUstreamCigCaptureParams* streamCigCaptureParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

1991 return _driver._cuStreamBeginCaptureToCig(hStream, streamCigCaptureParams) 

1992  

1993  

1994cdef CUresult cuStreamEndCaptureToCig(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil: 

1995 return _driver._cuStreamEndCaptureToCig(hStream) 

1996  

1997  

1998cdef CUresult cuFuncGetParamCount(CUfunction func, size_t* paramCount) except ?CUDA_ERROR_NOT_FOUND nogil: 

1999 return _driver._cuFuncGetParamCount(func, paramCount) 

2000  

2001  

2002cdef CUresult cuLaunchHostFunc_v2(CUstream hStream, CUhostFn fn, void* userData, unsigned int syncMode) except ?CUDA_ERROR_NOT_FOUND nogil: 

2003 return _driver._cuLaunchHostFunc_v2(hStream, fn, userData, syncMode) 

2004  

2005  

2006cdef CUresult cuGraphNodeGetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

2007 return _driver._cuGraphNodeGetParams(hNode, nodeParams) 21c2c3c4c#b$b%b'b]fGbHbIbacbcccdcec5c6cMbNbObicjcK L F c g h i kclc6

2008  

2009  

2010cdef CUresult cuCoredumpRegisterStartCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil: 

2011 return _driver._cuCoredumpRegisterStartCallback(callback, userData, callbackOut) 

2012  

2013  

2014cdef CUresult cuCoredumpRegisterCompleteCallback(CUcoredumpStatusCallback callback, void* userData, CUcoredumpCallbackHandle* callbackOut) except ?CUDA_ERROR_NOT_FOUND nogil: 

2015 return _driver._cuCoredumpRegisterCompleteCallback(callback, userData, callbackOut) 

2016  

2017  

2018cdef CUresult cuCoredumpDeregisterStartCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

2019 return _driver._cuCoredumpDeregisterStartCallback(callback) 

2020  

2021  

2022cdef CUresult cuCoredumpDeregisterCompleteCallback(CUcoredumpCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil: 

2023 return _driver._cuCoredumpDeregisterCompleteCallback(callback) 

2024  

2025  

2026cdef CUresult cuLogicalEndpointIdReserve(CUlogicalEndpointId* baseLeId, cuuint32_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

2027 return _driver._cuLogicalEndpointIdReserve(baseLeId, count) 

2028  

2029  

2030cdef CUresult cuLogicalEndpointIdRelease(CUlogicalEndpointId baseLeId, cuuint32_t count) except ?CUDA_ERROR_NOT_FOUND nogil: 

2031 return _driver._cuLogicalEndpointIdRelease(baseLeId, count) 

2032  

2033  

2034cdef CUresult cuLogicalEndpointCreate(CUlogicalEndpointId leId, const CUlogicalEndpointProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil: 

2035 return _driver._cuLogicalEndpointCreate(leId, prop) 

2036  

2037  

2038cdef CUresult cuLogicalEndpointAddDevice(CUlogicalEndpointId leId, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

2039 return _driver._cuLogicalEndpointAddDevice(leId, dev) 

2040  

2041  

2042cdef CUresult cuLogicalEndpointDestroy(CUlogicalEndpointId leId) except ?CUDA_ERROR_NOT_FOUND nogil: 

2043 return _driver._cuLogicalEndpointDestroy(leId) 

2044  

2045  

2046cdef CUresult cuLogicalEndpointBindAddr(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, void* ptr, cuuint64_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

2047 return _driver._cuLogicalEndpointBindAddr(leId, dev, offset, ptr, size, flags) 

2048  

2049  

2050cdef CUresult cuLogicalEndpointBindMem(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, CUmemGenericAllocationHandle memHandle, cuuint64_t memOffset, cuuint64_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil: 

2051 return _driver._cuLogicalEndpointBindMem(leId, dev, offset, memHandle, memOffset, size, flags) 

2052  

2053  

2054cdef CUresult cuLogicalEndpointUnbind(CUlogicalEndpointId leId, CUdevice dev, cuuint64_t offset, cuuint64_t size) except ?CUDA_ERROR_NOT_FOUND nogil: 

2055 return _driver._cuLogicalEndpointUnbind(leId, dev, offset, size) 

2056  

2057  

2058cdef CUresult cuLogicalEndpointExport(void* handle, CUlogicalEndpointId leId, CUlogicalEndpointIpcHandleType handleType) except ?CUDA_ERROR_NOT_FOUND nogil: 

2059 return _driver._cuLogicalEndpointExport(handle, leId, handleType) 

2060  

2061  

2062cdef CUresult cuLogicalEndpointImport(CUlogicalEndpointId leId, const void* handle, CUlogicalEndpointIpcHandleType handleType) except ?CUDA_ERROR_NOT_FOUND nogil: 

2063 return _driver._cuLogicalEndpointImport(leId, handle, handleType) 

2064  

2065  

2066cdef CUresult cuLogicalEndpointGetLimits(cuuint64_t* bindAlignment, cuuint64_t* maxSize, const CUlogicalEndpointProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil: 

2067 return _driver._cuLogicalEndpointGetLimits(bindAlignment, maxSize, prop) 

2068  

2069  

2070cdef CUresult cuLogicalEndpointQuery(CUlogicalEndpointId leId, cuuint32_t count, int* queryStatus) except ?CUDA_ERROR_NOT_FOUND nogil: 

2071 return _driver._cuLogicalEndpointQuery(leId, count, queryStatus) 

2072  

2073  

2074cdef CUresult cuStreamBeginRecaptureToGraph(CUstream hStream, CUstreamCaptureMode mode, CUgraph hGraph, CUgraphRecaptureCallback callbackFunc, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil: 

2075 return _driver._cuStreamBeginRecaptureToGraph(hStream, mode, hGraph, callbackFunc, userData) 

2076  

2077  

2078cdef CUresult cuDeviceGetFabricClusterUuid(CUuuid* uuid, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

2079 return _driver._cuDeviceGetFabricClusterUuid(uuid, dev) 

2080  

2081  

2082cdef CUresult cuDeviceGetCliqueCount(size_t* count, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

2083 return _driver._cuDeviceGetCliqueCount(count, dev) 

2084  

2085  

2086cdef CUresult cuDeviceGetCliqueInfo(CUcliqueInfo* cliqueInfo, size_t* count, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil: 

2087 return _driver._cuDeviceGetCliqueInfo(cliqueInfo, count, dev) 

2088  

2089  

2090cdef CUresult cuMemGetLocationInfo(CUdeviceptr ptr, size_t size, size_t summaryGranularity, size_t samplingGranularity, CUmemLocation* location_out) except ?CUDA_ERROR_NOT_FOUND nogil: 

2091 return _driver._cuMemGetLocationInfo(ptr, size, summaryGranularity, samplingGranularity, location_out) 

2092  

2093  

2094cdef CUresult cuGraphAddNode_v3(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

2095 return _driver._cuGraphAddNode_v3(phGraphNode, hGraph, dependencies, dependencyData, numDependencies, nodeParams) 

2096  

2097  

2098cdef CUresult cuGraphNodeSetParams_v2(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil: 

2099 return _driver._cuGraphNodeSetParams_v2(hNode, nodeParams) 

2100  

2101  

2102cdef CUresult cuCheckpointOperationComplete(CUcheckpointOperationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil: 

2103 return _driver._cuCheckpointOperationComplete(handle)