File size: 158,239 Bytes
76f9669 | 1 2 3 4 5 6 7 8 9 10 11 12 13 14 15 16 17 18 19 20 21 22 23 24 25 26 27 28 29 30 31 32 33 34 35 36 37 38 39 40 41 42 43 44 45 46 47 48 49 50 51 52 53 54 55 56 57 58 59 60 61 62 63 64 65 66 67 68 69 70 71 72 73 74 75 76 77 78 79 80 81 82 83 84 85 86 87 88 89 90 91 92 93 94 95 96 97 98 99 100 101 102 103 104 105 106 107 108 109 110 111 112 113 114 115 116 117 118 119 120 121 122 123 124 125 126 127 128 129 130 131 132 133 134 135 136 137 138 139 140 141 142 143 144 145 146 147 148 149 150 151 152 153 154 155 156 157 158 159 160 161 162 163 164 165 166 167 168 169 170 171 172 173 174 175 176 177 178 179 180 181 182 183 184 185 186 187 188 189 190 191 192 193 194 195 196 197 198 199 200 201 202 203 204 205 206 207 208 209 210 211 212 213 214 215 216 217 218 219 220 221 222 223 224 225 226 227 228 229 230 231 232 233 234 235 236 237 238 239 240 241 242 243 244 245 246 247 248 249 250 251 252 253 254 255 256 257 258 259 260 261 262 263 264 265 266 267 268 269 270 271 272 273 274 275 276 277 278 279 280 281 282 283 284 285 286 287 288 289 290 291 292 293 294 295 296 297 298 299 300 301 302 303 304 305 306 307 308 309 310 311 312 313 314 315 316 317 318 319 320 321 322 323 324 325 326 327 328 329 330 331 332 333 334 335 336 337 338 339 340 341 342 343 344 345 346 347 348 349 350 351 352 353 354 355 356 357 358 359 360 361 362 363 364 365 366 367 368 369 370 371 372 373 374 375 376 377 378 379 380 381 382 383 384 385 386 387 388 389 390 391 392 393 394 395 396 397 398 399 400 401 402 403 404 405 406 407 408 409 410 411 412 413 414 415 416 417 418 419 420 421 422 423 424 425 426 427 428 429 430 431 432 433 434 435 436 437 438 439 440 441 442 443 444 445 446 447 448 449 450 451 452 453 454 455 456 457 458 459 460 461 462 463 464 465 466 467 468 469 470 471 472 473 474 475 476 477 478 479 480 481 482 483 484 485 486 487 488 489 490 491 492 493 494 495 496 497 498 499 500 501 502 503 504 505 506 507 508 509 510 511 512 513 514 515 516 517 518 519 520 521 522 523 524 525 526 527 528 529 530 531 532 533 534 535 536 537 538 539 540 541 542 543 544 545 546 547 548 549 550 551 552 553 554 555 556 557 558 559 560 561 562 563 564 565 566 567 568 569 570 571 572 573 574 575 576 577 578 579 580 581 582 583 584 585 586 587 588 589 590 591 592 593 594 595 596 597 598 599 600 601 602 603 604 605 606 607 608 609 610 611 612 613 614 615 616 617 618 619 620 621 622 623 624 625 626 627 628 629 630 631 632 633 634 635 636 637 638 639 640 641 642 643 644 645 646 647 648 649 650 651 652 653 654 655 656 657 658 659 660 661 662 663 664 665 666 667 668 669 670 671 672 673 674 675 676 677 678 679 680 681 682 683 684 685 686 687 688 689 690 691 692 693 694 695 696 697 698 699 700 701 702 703 704 705 706 707 708 709 710 711 712 713 714 715 716 717 718 719 720 721 722 723 724 725 726 727 728 729 730 731 732 733 734 735 736 737 738 739 740 741 742 743 744 745 746 747 748 749 750 751 752 753 754 755 756 757 758 759 760 761 762 763 764 765 766 767 768 769 770 771 772 773 774 775 776 777 778 779 780 781 782 783 784 785 786 787 788 789 790 791 792 793 794 795 796 797 798 799 800 801 802 803 804 805 806 807 808 809 810 811 812 813 814 815 816 817 818 819 820 821 822 823 824 825 826 827 828 829 830 831 832 833 834 835 836 837 838 839 840 841 842 843 844 845 846 847 848 849 850 851 852 853 854 855 856 857 858 859 860 861 862 863 864 865 866 867 868 869 870 871 872 873 874 875 876 877 878 879 880 881 882 883 884 885 886 887 888 889 890 891 892 893 894 895 896 897 898 899 900 901 902 903 904 905 906 907 908 909 910 911 912 913 914 915 916 917 918 919 920 921 922 923 924 925 926 927 928 929 930 931 932 933 934 935 936 937 938 939 940 941 942 943 944 945 946 947 948 949 950 951 952 953 954 955 956 957 958 959 960 961 962 963 964 965 966 967 968 969 970 971 972 973 974 975 976 977 978 979 980 981 982 983 984 985 986 987 988 989 990 991 992 993 994 995 996 997 998 999 1000 1001 1002 1003 1004 1005 1006 1007 1008 1009 1010 1011 1012 1013 1014 1015 1016 1017 1018 1019 1020 1021 1022 1023 1024 1025 1026 1027 1028 1029 1030 1031 1032 1033 1034 1035 1036 1037 1038 1039 1040 1041 1042 1043 1044 1045 1046 1047 1048 1049 1050 1051 1052 1053 1054 1055 1056 1057 1058 1059 1060 1061 1062 1063 1064 1065 1066 1067 1068 1069 1070 1071 1072 1073 1074 1075 1076 1077 1078 1079 1080 1081 1082 1083 1084 1085 1086 1087 1088 1089 1090 1091 1092 1093 1094 1095 1096 1097 1098 1099 1100 1101 1102 1103 1104 1105 1106 1107 1108 1109 1110 1111 1112 1113 1114 1115 1116 1117 1118 1119 1120 1121 1122 1123 1124 1125 1126 1127 1128 1129 1130 1131 1132 1133 1134 1135 1136 1137 1138 1139 1140 1141 1142 1143 1144 1145 1146 1147 1148 1149 1150 1151 1152 1153 1154 1155 1156 1157 1158 1159 1160 1161 1162 1163 1164 1165 1166 1167 1168 1169 1170 1171 1172 1173 1174 1175 1176 1177 1178 1179 1180 1181 1182 1183 1184 1185 1186 1187 1188 1189 1190 1191 1192 1193 1194 1195 1196 1197 1198 1199 1200 1201 1202 1203 1204 1205 1206 1207 1208 1209 1210 1211 1212 1213 1214 1215 1216 1217 1218 1219 1220 1221 1222 1223 1224 1225 1226 1227 1228 1229 1230 1231 1232 1233 1234 1235 1236 1237 1238 1239 1240 1241 1242 1243 1244 1245 1246 1247 1248 1249 1250 1251 1252 1253 1254 1255 1256 1257 1258 1259 1260 1261 1262 1263 1264 1265 1266 1267 1268 1269 1270 1271 1272 1273 1274 1275 1276 1277 1278 1279 1280 1281 1282 1283 1284 1285 1286 1287 1288 1289 1290 1291 1292 1293 1294 1295 1296 1297 1298 1299 1300 1301 1302 1303 1304 1305 1306 1307 1308 1309 1310 1311 1312 1313 1314 1315 1316 1317 1318 1319 1320 1321 1322 1323 1324 1325 1326 1327 1328 1329 1330 1331 1332 1333 1334 1335 1336 1337 1338 1339 1340 1341 1342 1343 1344 1345 1346 1347 1348 1349 1350 1351 1352 1353 1354 1355 1356 1357 1358 1359 1360 1361 1362 1363 1364 1365 1366 1367 1368 1369 1370 1371 1372 1373 1374 1375 1376 1377 1378 1379 1380 1381 1382 1383 1384 1385 1386 1387 1388 1389 1390 1391 1392 1393 1394 1395 1396 1397 1398 1399 1400 1401 1402 1403 1404 1405 1406 1407 1408 1409 1410 1411 1412 1413 1414 1415 1416 1417 1418 1419 1420 1421 1422 1423 1424 1425 1426 1427 1428 1429 1430 1431 1432 1433 1434 1435 1436 1437 1438 1439 1440 1441 1442 1443 1444 1445 1446 1447 1448 1449 1450 1451 1452 1453 1454 1455 1456 1457 1458 1459 1460 1461 1462 1463 1464 1465 1466 1467 1468 1469 1470 1471 1472 1473 1474 1475 1476 1477 1478 1479 1480 1481 1482 1483 1484 1485 1486 1487 1488 1489 1490 1491 1492 1493 1494 1495 1496 1497 1498 1499 1500 1501 1502 1503 1504 1505 1506 1507 1508 1509 1510 1511 1512 1513 1514 1515 1516 1517 1518 1519 1520 1521 1522 1523 1524 1525 1526 1527 1528 1529 1530 1531 1532 1533 1534 1535 1536 1537 1538 1539 1540 1541 1542 1543 1544 1545 1546 1547 1548 1549 1550 1551 1552 1553 1554 1555 1556 1557 1558 1559 1560 1561 1562 1563 1564 1565 1566 1567 1568 1569 1570 1571 1572 1573 1574 1575 1576 1577 1578 1579 1580 1581 1582 1583 1584 1585 1586 1587 1588 1589 1590 1591 1592 1593 1594 1595 1596 1597 1598 1599 1600 1601 1602 1603 1604 1605 1606 1607 1608 1609 1610 1611 1612 1613 1614 1615 1616 1617 1618 1619 1620 1621 1622 1623 1624 1625 1626 1627 1628 1629 1630 1631 1632 1633 1634 1635 1636 1637 1638 1639 1640 1641 1642 1643 1644 1645 1646 1647 1648 1649 1650 1651 1652 1653 1654 1655 1656 1657 1658 1659 1660 1661 1662 1663 1664 1665 1666 1667 1668 1669 1670 1671 1672 1673 1674 1675 1676 1677 1678 1679 1680 1681 1682 1683 1684 1685 1686 1687 1688 1689 1690 1691 1692 1693 1694 1695 1696 1697 1698 1699 1700 1701 1702 1703 1704 1705 1706 1707 1708 1709 1710 1711 1712 1713 1714 1715 1716 1717 1718 1719 1720 1721 1722 1723 1724 1725 1726 1727 1728 1729 1730 1731 1732 1733 1734 1735 1736 1737 1738 1739 1740 1741 1742 1743 1744 1745 1746 1747 1748 1749 1750 1751 1752 1753 1754 1755 1756 1757 1758 1759 1760 1761 1762 1763 1764 1765 1766 1767 1768 1769 1770 1771 1772 1773 1774 1775 1776 1777 1778 1779 1780 1781 1782 1783 1784 1785 1786 1787 1788 1789 1790 1791 1792 1793 1794 1795 1796 1797 1798 1799 1800 1801 1802 1803 1804 1805 1806 1807 1808 1809 1810 1811 1812 1813 1814 1815 1816 1817 1818 1819 1820 1821 1822 1823 1824 1825 1826 1827 1828 1829 1830 1831 1832 1833 1834 1835 1836 1837 1838 1839 1840 1841 1842 1843 1844 1845 1846 1847 1848 1849 1850 1851 1852 1853 1854 1855 1856 1857 1858 1859 1860 1861 1862 1863 1864 1865 1866 1867 1868 1869 1870 1871 1872 1873 1874 1875 1876 1877 1878 1879 1880 1881 1882 1883 1884 1885 1886 1887 1888 1889 1890 1891 1892 1893 1894 1895 1896 1897 1898 1899 1900 1901 1902 1903 1904 1905 1906 1907 1908 1909 1910 1911 1912 1913 1914 1915 1916 1917 1918 1919 1920 1921 1922 1923 1924 1925 1926 1927 1928 1929 1930 1931 1932 1933 1934 1935 1936 1937 1938 1939 1940 1941 1942 1943 1944 1945 1946 1947 1948 1949 1950 1951 1952 1953 1954 1955 1956 1957 1958 1959 1960 1961 1962 1963 1964 1965 1966 1967 1968 1969 1970 1971 1972 1973 1974 1975 1976 1977 1978 1979 1980 1981 1982 1983 1984 1985 1986 1987 1988 1989 1990 1991 1992 1993 1994 1995 1996 1997 1998 1999 2000 2001 2002 2003 2004 2005 2006 2007 2008 2009 2010 2011 2012 2013 2014 2015 2016 2017 2018 2019 2020 2021 2022 2023 2024 2025 2026 2027 2028 2029 2030 2031 2032 2033 2034 2035 2036 2037 2038 2039 2040 2041 2042 2043 2044 2045 2046 2047 2048 2049 2050 2051 2052 2053 2054 2055 2056 2057 2058 2059 2060 2061 2062 2063 2064 2065 2066 2067 2068 2069 2070 2071 2072 2073 2074 2075 2076 2077 2078 2079 2080 2081 2082 2083 2084 2085 2086 2087 2088 2089 2090 2091 2092 2093 2094 2095 2096 2097 2098 2099 2100 2101 2102 2103 2104 2105 2106 2107 2108 2109 2110 2111 2112 2113 2114 2115 2116 2117 2118 2119 2120 2121 2122 2123 2124 2125 2126 2127 2128 2129 2130 2131 2132 2133 2134 2135 2136 2137 2138 2139 2140 2141 2142 2143 2144 2145 2146 2147 2148 2149 2150 2151 2152 2153 2154 2155 2156 2157 2158 2159 2160 2161 2162 2163 2164 2165 2166 2167 2168 2169 2170 2171 2172 2173 2174 2175 2176 2177 2178 2179 2180 2181 2182 2183 2184 2185 2186 2187 2188 2189 2190 2191 2192 2193 2194 2195 2196 2197 2198 2199 2200 2201 2202 2203 2204 2205 2206 2207 2208 2209 2210 2211 2212 2213 2214 2215 2216 2217 2218 2219 2220 2221 2222 2223 2224 2225 2226 2227 2228 2229 2230 2231 2232 2233 2234 2235 2236 2237 2238 2239 2240 2241 2242 2243 2244 2245 2246 2247 2248 2249 2250 2251 2252 2253 2254 2255 2256 2257 2258 2259 2260 2261 2262 2263 2264 2265 2266 2267 2268 2269 2270 2271 2272 2273 2274 2275 2276 2277 2278 2279 2280 2281 2282 2283 2284 2285 2286 2287 2288 2289 2290 2291 2292 2293 2294 2295 2296 2297 2298 2299 2300 2301 2302 2303 2304 2305 2306 2307 2308 2309 2310 2311 2312 2313 2314 2315 2316 2317 2318 2319 2320 2321 2322 2323 2324 2325 2326 2327 2328 2329 2330 2331 2332 2333 2334 2335 2336 2337 2338 2339 2340 2341 2342 2343 2344 2345 2346 2347 2348 2349 2350 2351 2352 2353 2354 2355 2356 2357 2358 2359 2360 2361 2362 2363 2364 2365 2366 2367 2368 2369 2370 2371 2372 2373 2374 2375 2376 2377 2378 2379 2380 2381 2382 2383 2384 2385 2386 2387 2388 2389 2390 2391 2392 2393 2394 2395 2396 2397 2398 2399 2400 2401 2402 2403 2404 2405 2406 2407 2408 2409 2410 2411 2412 2413 2414 2415 2416 2417 2418 2419 2420 2421 2422 2423 2424 2425 2426 2427 2428 2429 2430 2431 2432 2433 2434 2435 2436 2437 2438 2439 2440 2441 2442 2443 2444 2445 2446 2447 2448 2449 2450 2451 2452 2453 2454 2455 2456 2457 2458 2459 2460 2461 2462 2463 2464 2465 2466 2467 2468 2469 2470 2471 2472 2473 2474 2475 2476 2477 2478 2479 2480 2481 2482 2483 2484 2485 2486 2487 2488 2489 2490 2491 2492 2493 2494 2495 2496 2497 2498 2499 2500 2501 2502 2503 2504 2505 2506 2507 2508 2509 2510 2511 2512 2513 2514 2515 2516 2517 2518 2519 2520 2521 2522 2523 2524 2525 2526 2527 2528 2529 2530 2531 2532 2533 2534 2535 2536 2537 2538 2539 2540 2541 2542 2543 2544 2545 2546 2547 2548 2549 2550 2551 2552 2553 2554 2555 2556 2557 2558 2559 2560 2561 2562 2563 2564 2565 2566 2567 2568 2569 2570 2571 2572 2573 2574 2575 2576 2577 2578 2579 2580 2581 2582 2583 2584 2585 2586 2587 2588 2589 2590 2591 2592 2593 2594 2595 2596 2597 2598 2599 2600 2601 2602 2603 2604 2605 2606 2607 2608 2609 2610 2611 2612 2613 2614 2615 2616 2617 2618 2619 2620 2621 2622 2623 2624 2625 2626 2627 2628 2629 2630 2631 2632 2633 2634 2635 2636 2637 2638 2639 2640 2641 2642 2643 2644 2645 2646 2647 2648 2649 2650 2651 2652 2653 2654 2655 2656 2657 2658 2659 2660 2661 2662 2663 2664 2665 2666 2667 2668 2669 2670 2671 2672 2673 2674 2675 2676 2677 2678 2679 2680 2681 2682 2683 2684 2685 2686 2687 2688 2689 2690 2691 2692 2693 2694 2695 2696 2697 2698 2699 2700 2701 2702 2703 2704 2705 2706 2707 2708 2709 2710 2711 2712 2713 2714 2715 2716 2717 2718 2719 2720 2721 2722 2723 2724 2725 2726 2727 2728 2729 2730 2731 2732 2733 2734 2735 2736 2737 2738 2739 2740 2741 2742 2743 2744 2745 2746 2747 2748 2749 2750 2751 2752 2753 2754 2755 2756 2757 2758 2759 2760 2761 2762 2763 2764 2765 2766 2767 2768 2769 2770 2771 2772 2773 2774 2775 2776 2777 2778 2779 2780 2781 2782 2783 2784 2785 2786 2787 2788 2789 2790 2791 2792 2793 2794 2795 2796 2797 2798 2799 2800 2801 2802 2803 2804 2805 2806 2807 2808 2809 2810 2811 2812 2813 2814 2815 2816 2817 2818 2819 2820 2821 2822 2823 2824 2825 2826 2827 2828 2829 2830 2831 2832 2833 2834 2835 2836 2837 2838 2839 2840 2841 2842 2843 2844 2845 2846 2847 2848 2849 2850 2851 2852 2853 2854 2855 2856 2857 2858 2859 2860 2861 2862 2863 2864 2865 2866 2867 2868 2869 2870 2871 2872 2873 2874 2875 2876 2877 2878 2879 2880 2881 2882 2883 2884 2885 2886 2887 2888 2889 2890 2891 2892 2893 2894 2895 2896 2897 2898 2899 2900 2901 2902 2903 2904 2905 2906 2907 2908 2909 2910 2911 2912 2913 2914 2915 2916 2917 2918 2919 2920 2921 2922 2923 2924 2925 2926 2927 2928 2929 2930 2931 2932 2933 2934 2935 2936 2937 2938 2939 2940 2941 2942 2943 2944 2945 2946 2947 2948 2949 2950 2951 2952 2953 2954 2955 2956 2957 2958 2959 2960 2961 2962 2963 2964 2965 2966 2967 2968 2969 2970 2971 2972 2973 2974 2975 2976 2977 2978 2979 2980 2981 2982 2983 2984 2985 2986 2987 2988 2989 2990 2991 2992 2993 2994 2995 2996 2997 2998 2999 3000 3001 3002 3003 3004 3005 3006 3007 3008 3009 3010 3011 3012 3013 3014 3015 3016 3017 3018 3019 3020 3021 3022 3023 3024 3025 3026 3027 3028 3029 3030 3031 3032 3033 3034 3035 3036 3037 3038 3039 3040 3041 3042 3043 3044 3045 3046 3047 3048 3049 3050 3051 3052 3053 3054 3055 3056 3057 3058 3059 3060 3061 3062 3063 3064 3065 3066 3067 3068 3069 3070 3071 3072 3073 3074 3075 3076 3077 3078 3079 3080 3081 3082 3083 3084 3085 3086 3087 3088 3089 3090 3091 3092 3093 3094 3095 3096 3097 3098 3099 3100 3101 3102 3103 3104 3105 3106 3107 3108 3109 3110 3111 3112 3113 3114 3115 3116 3117 3118 3119 3120 3121 3122 3123 3124 3125 3126 3127 3128 3129 3130 3131 3132 3133 3134 3135 3136 3137 3138 3139 3140 3141 3142 3143 3144 3145 3146 3147 3148 3149 3150 3151 3152 3153 3154 3155 3156 3157 3158 3159 3160 3161 3162 3163 3164 3165 3166 3167 3168 3169 3170 3171 3172 3173 3174 3175 3176 3177 3178 3179 3180 3181 3182 3183 3184 3185 3186 3187 3188 3189 3190 3191 3192 3193 3194 3195 3196 3197 3198 3199 3200 3201 3202 3203 3204 3205 3206 3207 3208 3209 3210 3211 3212 3213 3214 3215 3216 3217 3218 3219 3220 3221 3222 3223 3224 3225 3226 3227 3228 3229 3230 3231 3232 3233 3234 3235 3236 3237 3238 3239 3240 3241 3242 3243 3244 3245 3246 3247 3248 3249 3250 3251 3252 3253 3254 3255 3256 3257 3258 3259 3260 3261 3262 3263 3264 3265 3266 3267 3268 3269 3270 3271 3272 3273 3274 3275 3276 3277 3278 3279 3280 3281 3282 3283 3284 3285 3286 3287 3288 3289 3290 3291 3292 3293 3294 3295 3296 3297 3298 3299 3300 3301 3302 3303 3304 3305 3306 3307 3308 3309 3310 3311 3312 3313 3314 3315 3316 3317 3318 3319 3320 3321 3322 3323 3324 3325 3326 3327 3328 3329 3330 3331 3332 3333 3334 3335 3336 3337 3338 3339 3340 3341 3342 3343 3344 3345 3346 3347 3348 3349 3350 3351 3352 3353 3354 3355 3356 3357 3358 3359 3360 3361 3362 3363 3364 3365 3366 3367 3368 3369 3370 3371 3372 3373 3374 3375 3376 3377 3378 3379 3380 3381 3382 3383 3384 3385 3386 3387 3388 3389 3390 3391 3392 3393 3394 3395 3396 3397 3398 3399 3400 3401 3402 3403 3404 3405 3406 3407 3408 3409 3410 3411 3412 3413 3414 3415 3416 3417 3418 3419 3420 3421 3422 3423 3424 3425 3426 3427 3428 3429 3430 3431 3432 3433 3434 3435 3436 3437 3438 3439 3440 3441 3442 3443 3444 3445 3446 3447 3448 3449 3450 3451 3452 3453 3454 3455 3456 3457 3458 3459 3460 3461 3462 3463 3464 3465 3466 3467 3468 3469 3470 3471 3472 3473 3474 3475 3476 3477 3478 3479 3480 3481 3482 3483 3484 3485 3486 3487 3488 3489 3490 3491 3492 3493 3494 3495 3496 3497 3498 3499 3500 3501 3502 3503 3504 3505 3506 3507 3508 3509 3510 3511 3512 3513 3514 3515 3516 3517 3518 3519 3520 3521 3522 3523 3524 3525 3526 3527 3528 3529 3530 3531 3532 3533 3534 3535 3536 3537 3538 3539 3540 3541 3542 3543 3544 3545 3546 3547 3548 3549 3550 3551 3552 3553 3554 3555 3556 3557 3558 3559 3560 3561 3562 3563 3564 3565 3566 3567 3568 3569 3570 3571 3572 3573 3574 3575 3576 3577 3578 3579 3580 3581 3582 3583 3584 3585 3586 3587 3588 3589 3590 3591 3592 3593 3594 3595 3596 3597 3598 3599 3600 3601 3602 3603 3604 3605 3606 3607 3608 3609 3610 3611 3612 3613 3614 3615 3616 3617 3618 3619 3620 3621 3622 3623 3624 3625 3626 3627 3628 3629 3630 3631 3632 3633 3634 3635 3636 3637 3638 3639 3640 3641 3642 3643 3644 3645 3646 3647 3648 3649 3650 3651 3652 3653 3654 3655 3656 3657 3658 3659 3660 3661 3662 3663 3664 3665 3666 3667 3668 3669 3670 3671 3672 3673 3674 3675 3676 3677 3678 3679 3680 3681 3682 3683 3684 3685 3686 3687 3688 3689 3690 3691 3692 3693 3694 3695 3696 3697 3698 3699 3700 3701 3702 3703 3704 3705 3706 3707 3708 3709 3710 3711 3712 3713 3714 3715 3716 3717 3718 3719 3720 3721 3722 3723 | # SPDX-FileCopyrightText: Copyright (c) 2021-2025 NVIDIA CORPORATION & AFFILIATES. All rights reserved.
# SPDX-License-Identifier: LicenseRef-NVIDIA-SOFTWARE-LICENSE
# This code was automatically generated with version 12.9.0. Do not modify it directly.
from libc.stdint cimport uint32_t, uint64_t
cdef extern from "cuda.h":
ctypedef uint32_t cuuint32_t
ctypedef uint64_t cuuint64_t
ctypedef unsigned long long CUdeviceptr_v2
ctypedef CUdeviceptr_v2 CUdeviceptr
ctypedef int CUdevice_v1
ctypedef CUdevice_v1 CUdevice
cdef struct CUctx_st:
pass
ctypedef CUctx_st* CUcontext
cdef struct CUmod_st:
pass
ctypedef CUmod_st* CUmodule
cdef struct CUfunc_st:
pass
ctypedef CUfunc_st* CUfunction
cdef struct CUlib_st:
pass
ctypedef CUlib_st* CUlibrary
cdef struct CUkern_st:
pass
ctypedef CUkern_st* CUkernel
cdef struct CUarray_st:
pass
ctypedef CUarray_st* CUarray
cdef struct CUmipmappedArray_st:
pass
ctypedef CUmipmappedArray_st* CUmipmappedArray
cdef struct CUtexref_st:
pass
ctypedef CUtexref_st* CUtexref
cdef struct CUsurfref_st:
pass
ctypedef CUsurfref_st* CUsurfref
cdef struct CUevent_st:
pass
ctypedef CUevent_st* CUevent
cdef struct CUstream_st:
pass
ctypedef CUstream_st* CUstream
cdef struct CUgraphicsResource_st:
pass
ctypedef CUgraphicsResource_st* CUgraphicsResource
ctypedef unsigned long long CUtexObject_v1
ctypedef CUtexObject_v1 CUtexObject
ctypedef unsigned long long CUsurfObject_v1
ctypedef CUsurfObject_v1 CUsurfObject
cdef struct CUextMemory_st:
pass
ctypedef CUextMemory_st* CUexternalMemory
cdef struct CUextSemaphore_st:
pass
ctypedef CUextSemaphore_st* CUexternalSemaphore
cdef struct CUgraph_st:
pass
ctypedef CUgraph_st* CUgraph
cdef struct CUgraphNode_st:
pass
ctypedef CUgraphNode_st* CUgraphNode
cdef struct CUgraphExec_st:
pass
ctypedef CUgraphExec_st* CUgraphExec
cdef struct CUmemPoolHandle_st:
pass
ctypedef CUmemPoolHandle_st* CUmemoryPool
cdef struct CUuserObject_st:
pass
ctypedef CUuserObject_st* CUuserObject
ctypedef cuuint64_t CUgraphConditionalHandle
cdef struct CUgraphDeviceUpdatableNode_st:
pass
ctypedef CUgraphDeviceUpdatableNode_st* CUgraphDeviceNode
cdef struct CUasyncCallbackEntry_st:
pass
ctypedef CUasyncCallbackEntry_st* CUasyncCallbackHandle
cdef struct CUgreenCtx_st:
pass
ctypedef CUgreenCtx_st* CUgreenCtx
cdef struct CUuuid_st:
char bytes[16]
ctypedef CUuuid_st CUuuid
cdef struct CUmemFabricHandle_st:
unsigned char data[64]
ctypedef CUmemFabricHandle_st CUmemFabricHandle_v1
ctypedef CUmemFabricHandle_v1 CUmemFabricHandle
cdef struct CUipcEventHandle_st:
char reserved[64]
ctypedef CUipcEventHandle_st CUipcEventHandle_v1
ctypedef CUipcEventHandle_v1 CUipcEventHandle
cdef struct CUipcMemHandle_st:
char reserved[64]
ctypedef CUipcMemHandle_st CUipcMemHandle_v1
ctypedef CUipcMemHandle_v1 CUipcMemHandle
cdef enum CUipcMem_flags_enum:
CU_IPC_MEM_LAZY_ENABLE_PEER_ACCESS = 1
ctypedef CUipcMem_flags_enum CUipcMem_flags
cdef enum CUmemAttach_flags_enum:
CU_MEM_ATTACH_GLOBAL = 1
CU_MEM_ATTACH_HOST = 2
CU_MEM_ATTACH_SINGLE = 4
ctypedef CUmemAttach_flags_enum CUmemAttach_flags
cdef enum CUctx_flags_enum:
CU_CTX_SCHED_AUTO = 0
CU_CTX_SCHED_SPIN = 1
CU_CTX_SCHED_YIELD = 2
CU_CTX_SCHED_BLOCKING_SYNC = 4
CU_CTX_BLOCKING_SYNC = 4
CU_CTX_SCHED_MASK = 7
CU_CTX_MAP_HOST = 8
CU_CTX_LMEM_RESIZE_TO_MAX = 16
CU_CTX_COREDUMP_ENABLE = 32
CU_CTX_USER_COREDUMP_ENABLE = 64
CU_CTX_SYNC_MEMOPS = 128
CU_CTX_FLAGS_MASK = 255
ctypedef CUctx_flags_enum CUctx_flags
cdef enum CUevent_sched_flags_enum:
CU_EVENT_SCHED_AUTO = 0
CU_EVENT_SCHED_SPIN = 1
CU_EVENT_SCHED_YIELD = 2
CU_EVENT_SCHED_BLOCKING_SYNC = 4
ctypedef CUevent_sched_flags_enum CUevent_sched_flags
cdef enum cl_event_flags_enum:
NVCL_EVENT_SCHED_AUTO = 0
NVCL_EVENT_SCHED_SPIN = 1
NVCL_EVENT_SCHED_YIELD = 2
NVCL_EVENT_SCHED_BLOCKING_SYNC = 4
ctypedef cl_event_flags_enum cl_event_flags
cdef enum cl_context_flags_enum:
NVCL_CTX_SCHED_AUTO = 0
NVCL_CTX_SCHED_SPIN = 1
NVCL_CTX_SCHED_YIELD = 2
NVCL_CTX_SCHED_BLOCKING_SYNC = 4
ctypedef cl_context_flags_enum cl_context_flags
cdef enum CUstream_flags_enum:
CU_STREAM_DEFAULT = 0
CU_STREAM_NON_BLOCKING = 1
ctypedef CUstream_flags_enum CUstream_flags
cdef enum CUevent_flags_enum:
CU_EVENT_DEFAULT = 0
CU_EVENT_BLOCKING_SYNC = 1
CU_EVENT_DISABLE_TIMING = 2
CU_EVENT_INTERPROCESS = 4
ctypedef CUevent_flags_enum CUevent_flags
cdef enum CUevent_record_flags_enum:
CU_EVENT_RECORD_DEFAULT = 0
CU_EVENT_RECORD_EXTERNAL = 1
ctypedef CUevent_record_flags_enum CUevent_record_flags
cdef enum CUevent_wait_flags_enum:
CU_EVENT_WAIT_DEFAULT = 0
CU_EVENT_WAIT_EXTERNAL = 1
ctypedef CUevent_wait_flags_enum CUevent_wait_flags
cdef enum CUstreamWaitValue_flags_enum:
CU_STREAM_WAIT_VALUE_GEQ = 0
CU_STREAM_WAIT_VALUE_EQ = 1
CU_STREAM_WAIT_VALUE_AND = 2
CU_STREAM_WAIT_VALUE_NOR = 3
CU_STREAM_WAIT_VALUE_FLUSH = 1073741824
ctypedef CUstreamWaitValue_flags_enum CUstreamWaitValue_flags
cdef enum CUstreamWriteValue_flags_enum:
CU_STREAM_WRITE_VALUE_DEFAULT = 0
CU_STREAM_WRITE_VALUE_NO_MEMORY_BARRIER = 1
ctypedef CUstreamWriteValue_flags_enum CUstreamWriteValue_flags
cdef enum CUstreamBatchMemOpType_enum:
CU_STREAM_MEM_OP_WAIT_VALUE_32 = 1
CU_STREAM_MEM_OP_WRITE_VALUE_32 = 2
CU_STREAM_MEM_OP_FLUSH_REMOTE_WRITES = 3
CU_STREAM_MEM_OP_WAIT_VALUE_64 = 4
CU_STREAM_MEM_OP_WRITE_VALUE_64 = 5
CU_STREAM_MEM_OP_BARRIER = 6
ctypedef CUstreamBatchMemOpType_enum CUstreamBatchMemOpType
cdef enum CUstreamMemoryBarrier_flags_enum:
CU_STREAM_MEMORY_BARRIER_TYPE_SYS = 0
CU_STREAM_MEMORY_BARRIER_TYPE_GPU = 1
ctypedef CUstreamMemoryBarrier_flags_enum CUstreamMemoryBarrier_flags
cdef struct CUstreamMemOpWaitValueParams_st:
CUstreamBatchMemOpType operation
CUdeviceptr address
cuuint32_t value
cuuint64_t value64
unsigned int flags
CUdeviceptr alias
cdef struct CUstreamMemOpWriteValueParams_st:
CUstreamBatchMemOpType operation
CUdeviceptr address
cuuint32_t value
cuuint64_t value64
unsigned int flags
CUdeviceptr alias
cdef struct CUstreamMemOpFlushRemoteWritesParams_st:
CUstreamBatchMemOpType operation
unsigned int flags
cdef struct CUstreamMemOpMemoryBarrierParams_st:
CUstreamBatchMemOpType operation
unsigned int flags
cdef union CUstreamBatchMemOpParams_union:
CUstreamBatchMemOpType operation
CUstreamMemOpWaitValueParams_st waitValue
CUstreamMemOpWriteValueParams_st writeValue
CUstreamMemOpFlushRemoteWritesParams_st flushRemoteWrites
CUstreamMemOpMemoryBarrierParams_st memoryBarrier
cuuint64_t pad[6]
ctypedef CUstreamBatchMemOpParams_union CUstreamBatchMemOpParams_v1
ctypedef CUstreamBatchMemOpParams_v1 CUstreamBatchMemOpParams
cdef struct CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st:
CUcontext ctx
unsigned int count
CUstreamBatchMemOpParams* paramArray
unsigned int flags
ctypedef CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st CUDA_BATCH_MEM_OP_NODE_PARAMS_v1
ctypedef CUDA_BATCH_MEM_OP_NODE_PARAMS_v1 CUDA_BATCH_MEM_OP_NODE_PARAMS
cdef struct CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st:
CUcontext ctx
unsigned int count
CUstreamBatchMemOpParams* paramArray
unsigned int flags
ctypedef CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st CUDA_BATCH_MEM_OP_NODE_PARAMS_v2
cdef enum CUoccupancy_flags_enum:
CU_OCCUPANCY_DEFAULT = 0
CU_OCCUPANCY_DISABLE_CACHING_OVERRIDE = 1
ctypedef CUoccupancy_flags_enum CUoccupancy_flags
cdef enum CUstreamUpdateCaptureDependencies_flags_enum:
CU_STREAM_ADD_CAPTURE_DEPENDENCIES = 0
CU_STREAM_SET_CAPTURE_DEPENDENCIES = 1
ctypedef CUstreamUpdateCaptureDependencies_flags_enum CUstreamUpdateCaptureDependencies_flags
cdef enum CUasyncNotificationType_enum:
CU_ASYNC_NOTIFICATION_TYPE_OVER_BUDGET = 1
ctypedef CUasyncNotificationType_enum CUasyncNotificationType
cdef struct anon_struct0:
unsigned long long bytesOverBudget
cdef union anon_union2:
anon_struct0 overBudget
cdef struct CUasyncNotificationInfo_st:
CUasyncNotificationType type
anon_union2 info
ctypedef CUasyncNotificationInfo_st CUasyncNotificationInfo
ctypedef void (*CUasyncCallback)(CUasyncNotificationInfo* info, void* userData, CUasyncCallbackHandle callback)
cdef enum CUarray_format_enum:
CU_AD_FORMAT_UNSIGNED_INT8 = 1
CU_AD_FORMAT_UNSIGNED_INT16 = 2
CU_AD_FORMAT_UNSIGNED_INT32 = 3
CU_AD_FORMAT_SIGNED_INT8 = 8
CU_AD_FORMAT_SIGNED_INT16 = 9
CU_AD_FORMAT_SIGNED_INT32 = 10
CU_AD_FORMAT_HALF = 16
CU_AD_FORMAT_FLOAT = 32
CU_AD_FORMAT_UNORM_INT_101010_2 = 80
CU_AD_FORMAT_BC1_UNORM = 145
CU_AD_FORMAT_BC1_UNORM_SRGB = 146
CU_AD_FORMAT_BC2_UNORM = 147
CU_AD_FORMAT_BC2_UNORM_SRGB = 148
CU_AD_FORMAT_BC3_UNORM = 149
CU_AD_FORMAT_BC3_UNORM_SRGB = 150
CU_AD_FORMAT_BC4_UNORM = 151
CU_AD_FORMAT_BC4_SNORM = 152
CU_AD_FORMAT_BC5_UNORM = 153
CU_AD_FORMAT_BC5_SNORM = 154
CU_AD_FORMAT_BC6H_UF16 = 155
CU_AD_FORMAT_BC6H_SF16 = 156
CU_AD_FORMAT_BC7_UNORM = 157
CU_AD_FORMAT_BC7_UNORM_SRGB = 158
CU_AD_FORMAT_P010 = 159
CU_AD_FORMAT_P016 = 161
CU_AD_FORMAT_NV16 = 162
CU_AD_FORMAT_P210 = 163
CU_AD_FORMAT_P216 = 164
CU_AD_FORMAT_YUY2 = 165
CU_AD_FORMAT_Y210 = 166
CU_AD_FORMAT_Y216 = 167
CU_AD_FORMAT_AYUV = 168
CU_AD_FORMAT_Y410 = 169
CU_AD_FORMAT_NV12 = 176
CU_AD_FORMAT_Y416 = 177
CU_AD_FORMAT_Y444_PLANAR8 = 178
CU_AD_FORMAT_Y444_PLANAR10 = 179
CU_AD_FORMAT_YUV444_8bit_SemiPlanar = 180
CU_AD_FORMAT_YUV444_16bit_SemiPlanar = 181
CU_AD_FORMAT_UNORM_INT8X1 = 192
CU_AD_FORMAT_UNORM_INT8X2 = 193
CU_AD_FORMAT_UNORM_INT8X4 = 194
CU_AD_FORMAT_UNORM_INT16X1 = 195
CU_AD_FORMAT_UNORM_INT16X2 = 196
CU_AD_FORMAT_UNORM_INT16X4 = 197
CU_AD_FORMAT_SNORM_INT8X1 = 198
CU_AD_FORMAT_SNORM_INT8X2 = 199
CU_AD_FORMAT_SNORM_INT8X4 = 200
CU_AD_FORMAT_SNORM_INT16X1 = 201
CU_AD_FORMAT_SNORM_INT16X2 = 202
CU_AD_FORMAT_SNORM_INT16X4 = 203
CU_AD_FORMAT_MAX = 2147483647
ctypedef CUarray_format_enum CUarray_format
cdef enum CUaddress_mode_enum:
CU_TR_ADDRESS_MODE_WRAP = 0
CU_TR_ADDRESS_MODE_CLAMP = 1
CU_TR_ADDRESS_MODE_MIRROR = 2
CU_TR_ADDRESS_MODE_BORDER = 3
ctypedef CUaddress_mode_enum CUaddress_mode
cdef enum CUfilter_mode_enum:
CU_TR_FILTER_MODE_POINT = 0
CU_TR_FILTER_MODE_LINEAR = 1
ctypedef CUfilter_mode_enum CUfilter_mode
cdef enum CUdevice_attribute_enum:
CU_DEVICE_ATTRIBUTE_MAX_THREADS_PER_BLOCK = 1
CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_X = 2
CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_Y = 3
CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_Z = 4
CU_DEVICE_ATTRIBUTE_MAX_GRID_DIM_X = 5
CU_DEVICE_ATTRIBUTE_MAX_GRID_DIM_Y = 6
CU_DEVICE_ATTRIBUTE_MAX_GRID_DIM_Z = 7
CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_BLOCK = 8
CU_DEVICE_ATTRIBUTE_SHARED_MEMORY_PER_BLOCK = 8
CU_DEVICE_ATTRIBUTE_TOTAL_CONSTANT_MEMORY = 9
CU_DEVICE_ATTRIBUTE_WARP_SIZE = 10
CU_DEVICE_ATTRIBUTE_MAX_PITCH = 11
CU_DEVICE_ATTRIBUTE_MAX_REGISTERS_PER_BLOCK = 12
CU_DEVICE_ATTRIBUTE_REGISTERS_PER_BLOCK = 12
CU_DEVICE_ATTRIBUTE_CLOCK_RATE = 13
CU_DEVICE_ATTRIBUTE_TEXTURE_ALIGNMENT = 14
CU_DEVICE_ATTRIBUTE_GPU_OVERLAP = 15
CU_DEVICE_ATTRIBUTE_MULTIPROCESSOR_COUNT = 16
CU_DEVICE_ATTRIBUTE_KERNEL_EXEC_TIMEOUT = 17
CU_DEVICE_ATTRIBUTE_INTEGRATED = 18
CU_DEVICE_ATTRIBUTE_CAN_MAP_HOST_MEMORY = 19
CU_DEVICE_ATTRIBUTE_COMPUTE_MODE = 20
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE1D_WIDTH = 21
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_WIDTH = 22
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_HEIGHT = 23
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE3D_WIDTH = 24
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE3D_HEIGHT = 25
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE3D_DEPTH = 26
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_LAYERED_WIDTH = 27
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_ARRAY_WIDTH = 27
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_LAYERED_HEIGHT = 28
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_ARRAY_HEIGHT = 28
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_LAYERED_LAYERS = 29
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_ARRAY_NUMSLICES = 29
CU_DEVICE_ATTRIBUTE_SURFACE_ALIGNMENT = 30
CU_DEVICE_ATTRIBUTE_CONCURRENT_KERNELS = 31
CU_DEVICE_ATTRIBUTE_ECC_ENABLED = 32
CU_DEVICE_ATTRIBUTE_PCI_BUS_ID = 33
CU_DEVICE_ATTRIBUTE_PCI_DEVICE_ID = 34
CU_DEVICE_ATTRIBUTE_TCC_DRIVER = 35
CU_DEVICE_ATTRIBUTE_MEMORY_CLOCK_RATE = 36
CU_DEVICE_ATTRIBUTE_GLOBAL_MEMORY_BUS_WIDTH = 37
CU_DEVICE_ATTRIBUTE_L2_CACHE_SIZE = 38
CU_DEVICE_ATTRIBUTE_MAX_THREADS_PER_MULTIPROCESSOR = 39
CU_DEVICE_ATTRIBUTE_ASYNC_ENGINE_COUNT = 40
CU_DEVICE_ATTRIBUTE_UNIFIED_ADDRESSING = 41
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE1D_LAYERED_WIDTH = 42
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE1D_LAYERED_LAYERS = 43
CU_DEVICE_ATTRIBUTE_CAN_TEX2D_GATHER = 44
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_GATHER_WIDTH = 45
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_GATHER_HEIGHT = 46
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE3D_WIDTH_ALTERNATE = 47
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE3D_HEIGHT_ALTERNATE = 48
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE3D_DEPTH_ALTERNATE = 49
CU_DEVICE_ATTRIBUTE_PCI_DOMAIN_ID = 50
CU_DEVICE_ATTRIBUTE_TEXTURE_PITCH_ALIGNMENT = 51
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURECUBEMAP_WIDTH = 52
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURECUBEMAP_LAYERED_WIDTH = 53
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURECUBEMAP_LAYERED_LAYERS = 54
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE1D_WIDTH = 55
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE2D_WIDTH = 56
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE2D_HEIGHT = 57
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE3D_WIDTH = 58
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE3D_HEIGHT = 59
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE3D_DEPTH = 60
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE1D_LAYERED_WIDTH = 61
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE1D_LAYERED_LAYERS = 62
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE2D_LAYERED_WIDTH = 63
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE2D_LAYERED_HEIGHT = 64
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACE2D_LAYERED_LAYERS = 65
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACECUBEMAP_WIDTH = 66
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACECUBEMAP_LAYERED_WIDTH = 67
CU_DEVICE_ATTRIBUTE_MAXIMUM_SURFACECUBEMAP_LAYERED_LAYERS = 68
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE1D_LINEAR_WIDTH = 69
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_LINEAR_WIDTH = 70
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_LINEAR_HEIGHT = 71
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_LINEAR_PITCH = 72
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_MIPMAPPED_WIDTH = 73
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_MIPMAPPED_HEIGHT = 74
CU_DEVICE_ATTRIBUTE_COMPUTE_CAPABILITY_MAJOR = 75
CU_DEVICE_ATTRIBUTE_COMPUTE_CAPABILITY_MINOR = 76
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE1D_MIPMAPPED_WIDTH = 77
CU_DEVICE_ATTRIBUTE_STREAM_PRIORITIES_SUPPORTED = 78
CU_DEVICE_ATTRIBUTE_GLOBAL_L1_CACHE_SUPPORTED = 79
CU_DEVICE_ATTRIBUTE_LOCAL_L1_CACHE_SUPPORTED = 80
CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_MULTIPROCESSOR = 81
CU_DEVICE_ATTRIBUTE_MAX_REGISTERS_PER_MULTIPROCESSOR = 82
CU_DEVICE_ATTRIBUTE_MANAGED_MEMORY = 83
CU_DEVICE_ATTRIBUTE_MULTI_GPU_BOARD = 84
CU_DEVICE_ATTRIBUTE_MULTI_GPU_BOARD_GROUP_ID = 85
CU_DEVICE_ATTRIBUTE_HOST_NATIVE_ATOMIC_SUPPORTED = 86
CU_DEVICE_ATTRIBUTE_SINGLE_TO_DOUBLE_PRECISION_PERF_RATIO = 87
CU_DEVICE_ATTRIBUTE_PAGEABLE_MEMORY_ACCESS = 88
CU_DEVICE_ATTRIBUTE_CONCURRENT_MANAGED_ACCESS = 89
CU_DEVICE_ATTRIBUTE_COMPUTE_PREEMPTION_SUPPORTED = 90
CU_DEVICE_ATTRIBUTE_CAN_USE_HOST_POINTER_FOR_REGISTERED_MEM = 91
CU_DEVICE_ATTRIBUTE_CAN_USE_STREAM_MEM_OPS_V1 = 92
CU_DEVICE_ATTRIBUTE_CAN_USE_64_BIT_STREAM_MEM_OPS_V1 = 93
CU_DEVICE_ATTRIBUTE_CAN_USE_STREAM_WAIT_VALUE_NOR_V1 = 94
CU_DEVICE_ATTRIBUTE_COOPERATIVE_LAUNCH = 95
CU_DEVICE_ATTRIBUTE_COOPERATIVE_MULTI_DEVICE_LAUNCH = 96
CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_BLOCK_OPTIN = 97
CU_DEVICE_ATTRIBUTE_CAN_FLUSH_REMOTE_WRITES = 98
CU_DEVICE_ATTRIBUTE_HOST_REGISTER_SUPPORTED = 99
CU_DEVICE_ATTRIBUTE_PAGEABLE_MEMORY_ACCESS_USES_HOST_PAGE_TABLES = 100
CU_DEVICE_ATTRIBUTE_DIRECT_MANAGED_MEM_ACCESS_FROM_HOST = 101
CU_DEVICE_ATTRIBUTE_VIRTUAL_ADDRESS_MANAGEMENT_SUPPORTED = 102
CU_DEVICE_ATTRIBUTE_VIRTUAL_MEMORY_MANAGEMENT_SUPPORTED = 102
CU_DEVICE_ATTRIBUTE_HANDLE_TYPE_POSIX_FILE_DESCRIPTOR_SUPPORTED = 103
CU_DEVICE_ATTRIBUTE_HANDLE_TYPE_WIN32_HANDLE_SUPPORTED = 104
CU_DEVICE_ATTRIBUTE_HANDLE_TYPE_WIN32_KMT_HANDLE_SUPPORTED = 105
CU_DEVICE_ATTRIBUTE_MAX_BLOCKS_PER_MULTIPROCESSOR = 106
CU_DEVICE_ATTRIBUTE_GENERIC_COMPRESSION_SUPPORTED = 107
CU_DEVICE_ATTRIBUTE_MAX_PERSISTING_L2_CACHE_SIZE = 108
CU_DEVICE_ATTRIBUTE_MAX_ACCESS_POLICY_WINDOW_SIZE = 109
CU_DEVICE_ATTRIBUTE_GPU_DIRECT_RDMA_WITH_CUDA_VMM_SUPPORTED = 110
CU_DEVICE_ATTRIBUTE_RESERVED_SHARED_MEMORY_PER_BLOCK = 111
CU_DEVICE_ATTRIBUTE_SPARSE_CUDA_ARRAY_SUPPORTED = 112
CU_DEVICE_ATTRIBUTE_READ_ONLY_HOST_REGISTER_SUPPORTED = 113
CU_DEVICE_ATTRIBUTE_TIMELINE_SEMAPHORE_INTEROP_SUPPORTED = 114
CU_DEVICE_ATTRIBUTE_MEMORY_POOLS_SUPPORTED = 115
CU_DEVICE_ATTRIBUTE_GPU_DIRECT_RDMA_SUPPORTED = 116
CU_DEVICE_ATTRIBUTE_GPU_DIRECT_RDMA_FLUSH_WRITES_OPTIONS = 117
CU_DEVICE_ATTRIBUTE_GPU_DIRECT_RDMA_WRITES_ORDERING = 118
CU_DEVICE_ATTRIBUTE_MEMPOOL_SUPPORTED_HANDLE_TYPES = 119
CU_DEVICE_ATTRIBUTE_CLUSTER_LAUNCH = 120
CU_DEVICE_ATTRIBUTE_DEFERRED_MAPPING_CUDA_ARRAY_SUPPORTED = 121
CU_DEVICE_ATTRIBUTE_CAN_USE_64_BIT_STREAM_MEM_OPS = 122
CU_DEVICE_ATTRIBUTE_CAN_USE_STREAM_WAIT_VALUE_NOR = 123
CU_DEVICE_ATTRIBUTE_DMA_BUF_SUPPORTED = 124
CU_DEVICE_ATTRIBUTE_IPC_EVENT_SUPPORTED = 125
CU_DEVICE_ATTRIBUTE_MEM_SYNC_DOMAIN_COUNT = 126
CU_DEVICE_ATTRIBUTE_TENSOR_MAP_ACCESS_SUPPORTED = 127
CU_DEVICE_ATTRIBUTE_HANDLE_TYPE_FABRIC_SUPPORTED = 128
CU_DEVICE_ATTRIBUTE_UNIFIED_FUNCTION_POINTERS = 129
CU_DEVICE_ATTRIBUTE_NUMA_CONFIG = 130
CU_DEVICE_ATTRIBUTE_NUMA_ID = 131
CU_DEVICE_ATTRIBUTE_MULTICAST_SUPPORTED = 132
CU_DEVICE_ATTRIBUTE_MPS_ENABLED = 133
CU_DEVICE_ATTRIBUTE_HOST_NUMA_ID = 134
CU_DEVICE_ATTRIBUTE_D3D12_CIG_SUPPORTED = 135
CU_DEVICE_ATTRIBUTE_MEM_DECOMPRESS_ALGORITHM_MASK = 136
CU_DEVICE_ATTRIBUTE_MEM_DECOMPRESS_MAXIMUM_LENGTH = 137
CU_DEVICE_ATTRIBUTE_VULKAN_CIG_SUPPORTED = 138
CU_DEVICE_ATTRIBUTE_GPU_PCI_DEVICE_ID = 139
CU_DEVICE_ATTRIBUTE_GPU_PCI_SUBSYSTEM_ID = 140
CU_DEVICE_ATTRIBUTE_HOST_NUMA_VIRTUAL_MEMORY_MANAGEMENT_SUPPORTED = 141
CU_DEVICE_ATTRIBUTE_HOST_NUMA_MEMORY_POOLS_SUPPORTED = 142
CU_DEVICE_ATTRIBUTE_HOST_NUMA_MULTINODE_IPC_SUPPORTED = 143
CU_DEVICE_ATTRIBUTE_MAX = 144
ctypedef CUdevice_attribute_enum CUdevice_attribute
cdef struct CUdevprop_st:
int maxThreadsPerBlock
int maxThreadsDim[3]
int maxGridSize[3]
int sharedMemPerBlock
int totalConstantMemory
int SIMDWidth
int memPitch
int regsPerBlock
int clockRate
int textureAlign
ctypedef CUdevprop_st CUdevprop_v1
ctypedef CUdevprop_v1 CUdevprop
cdef enum CUpointer_attribute_enum:
CU_POINTER_ATTRIBUTE_CONTEXT = 1
CU_POINTER_ATTRIBUTE_MEMORY_TYPE = 2
CU_POINTER_ATTRIBUTE_DEVICE_POINTER = 3
CU_POINTER_ATTRIBUTE_HOST_POINTER = 4
CU_POINTER_ATTRIBUTE_P2P_TOKENS = 5
CU_POINTER_ATTRIBUTE_SYNC_MEMOPS = 6
CU_POINTER_ATTRIBUTE_BUFFER_ID = 7
CU_POINTER_ATTRIBUTE_IS_MANAGED = 8
CU_POINTER_ATTRIBUTE_DEVICE_ORDINAL = 9
CU_POINTER_ATTRIBUTE_IS_LEGACY_CUDA_IPC_CAPABLE = 10
CU_POINTER_ATTRIBUTE_RANGE_START_ADDR = 11
CU_POINTER_ATTRIBUTE_RANGE_SIZE = 12
CU_POINTER_ATTRIBUTE_MAPPED = 13
CU_POINTER_ATTRIBUTE_ALLOWED_HANDLE_TYPES = 14
CU_POINTER_ATTRIBUTE_IS_GPU_DIRECT_RDMA_CAPABLE = 15
CU_POINTER_ATTRIBUTE_ACCESS_FLAGS = 16
CU_POINTER_ATTRIBUTE_MEMPOOL_HANDLE = 17
CU_POINTER_ATTRIBUTE_MAPPING_SIZE = 18
CU_POINTER_ATTRIBUTE_MAPPING_BASE_ADDR = 19
CU_POINTER_ATTRIBUTE_MEMORY_BLOCK_ID = 20
CU_POINTER_ATTRIBUTE_IS_HW_DECOMPRESS_CAPABLE = 21
ctypedef CUpointer_attribute_enum CUpointer_attribute
cdef enum CUfunction_attribute_enum:
CU_FUNC_ATTRIBUTE_MAX_THREADS_PER_BLOCK = 0
CU_FUNC_ATTRIBUTE_SHARED_SIZE_BYTES = 1
CU_FUNC_ATTRIBUTE_CONST_SIZE_BYTES = 2
CU_FUNC_ATTRIBUTE_LOCAL_SIZE_BYTES = 3
CU_FUNC_ATTRIBUTE_NUM_REGS = 4
CU_FUNC_ATTRIBUTE_PTX_VERSION = 5
CU_FUNC_ATTRIBUTE_BINARY_VERSION = 6
CU_FUNC_ATTRIBUTE_CACHE_MODE_CA = 7
CU_FUNC_ATTRIBUTE_MAX_DYNAMIC_SHARED_SIZE_BYTES = 8
CU_FUNC_ATTRIBUTE_PREFERRED_SHARED_MEMORY_CARVEOUT = 9
CU_FUNC_ATTRIBUTE_CLUSTER_SIZE_MUST_BE_SET = 10
CU_FUNC_ATTRIBUTE_REQUIRED_CLUSTER_WIDTH = 11
CU_FUNC_ATTRIBUTE_REQUIRED_CLUSTER_HEIGHT = 12
CU_FUNC_ATTRIBUTE_REQUIRED_CLUSTER_DEPTH = 13
CU_FUNC_ATTRIBUTE_NON_PORTABLE_CLUSTER_SIZE_ALLOWED = 14
CU_FUNC_ATTRIBUTE_CLUSTER_SCHEDULING_POLICY_PREFERENCE = 15
CU_FUNC_ATTRIBUTE_MAX = 16
ctypedef CUfunction_attribute_enum CUfunction_attribute
cdef enum CUfunc_cache_enum:
CU_FUNC_CACHE_PREFER_NONE = 0
CU_FUNC_CACHE_PREFER_SHARED = 1
CU_FUNC_CACHE_PREFER_L1 = 2
CU_FUNC_CACHE_PREFER_EQUAL = 3
ctypedef CUfunc_cache_enum CUfunc_cache
cdef enum CUsharedconfig_enum:
CU_SHARED_MEM_CONFIG_DEFAULT_BANK_SIZE = 0
CU_SHARED_MEM_CONFIG_FOUR_BYTE_BANK_SIZE = 1
CU_SHARED_MEM_CONFIG_EIGHT_BYTE_BANK_SIZE = 2
ctypedef CUsharedconfig_enum CUsharedconfig
cdef enum CUshared_carveout_enum:
CU_SHAREDMEM_CARVEOUT_DEFAULT = -1
CU_SHAREDMEM_CARVEOUT_MAX_L1 = 0
CU_SHAREDMEM_CARVEOUT_MAX_SHARED = 100
ctypedef CUshared_carveout_enum CUshared_carveout
cdef enum CUmemorytype_enum:
CU_MEMORYTYPE_HOST = 1
CU_MEMORYTYPE_DEVICE = 2
CU_MEMORYTYPE_ARRAY = 3
CU_MEMORYTYPE_UNIFIED = 4
ctypedef CUmemorytype_enum CUmemorytype
cdef enum CUcomputemode_enum:
CU_COMPUTEMODE_DEFAULT = 0
CU_COMPUTEMODE_PROHIBITED = 2
CU_COMPUTEMODE_EXCLUSIVE_PROCESS = 3
ctypedef CUcomputemode_enum CUcomputemode
cdef enum CUmem_advise_enum:
CU_MEM_ADVISE_SET_READ_MOSTLY = 1
CU_MEM_ADVISE_UNSET_READ_MOSTLY = 2
CU_MEM_ADVISE_SET_PREFERRED_LOCATION = 3
CU_MEM_ADVISE_UNSET_PREFERRED_LOCATION = 4
CU_MEM_ADVISE_SET_ACCESSED_BY = 5
CU_MEM_ADVISE_UNSET_ACCESSED_BY = 6
ctypedef CUmem_advise_enum CUmem_advise
cdef enum CUmem_range_attribute_enum:
CU_MEM_RANGE_ATTRIBUTE_READ_MOSTLY = 1
CU_MEM_RANGE_ATTRIBUTE_PREFERRED_LOCATION = 2
CU_MEM_RANGE_ATTRIBUTE_ACCESSED_BY = 3
CU_MEM_RANGE_ATTRIBUTE_LAST_PREFETCH_LOCATION = 4
CU_MEM_RANGE_ATTRIBUTE_PREFERRED_LOCATION_TYPE = 5
CU_MEM_RANGE_ATTRIBUTE_PREFERRED_LOCATION_ID = 6
CU_MEM_RANGE_ATTRIBUTE_LAST_PREFETCH_LOCATION_TYPE = 7
CU_MEM_RANGE_ATTRIBUTE_LAST_PREFETCH_LOCATION_ID = 8
ctypedef CUmem_range_attribute_enum CUmem_range_attribute
cdef enum CUjit_option_enum:
CU_JIT_MAX_REGISTERS = 0
CU_JIT_THREADS_PER_BLOCK = 1
CU_JIT_WALL_TIME = 2
CU_JIT_INFO_LOG_BUFFER = 3
CU_JIT_INFO_LOG_BUFFER_SIZE_BYTES = 4
CU_JIT_ERROR_LOG_BUFFER = 5
CU_JIT_ERROR_LOG_BUFFER_SIZE_BYTES = 6
CU_JIT_OPTIMIZATION_LEVEL = 7
CU_JIT_TARGET_FROM_CUCONTEXT = 8
CU_JIT_TARGET = 9
CU_JIT_FALLBACK_STRATEGY = 10
CU_JIT_GENERATE_DEBUG_INFO = 11
CU_JIT_LOG_VERBOSE = 12
CU_JIT_GENERATE_LINE_INFO = 13
CU_JIT_CACHE_MODE = 14
CU_JIT_NEW_SM3X_OPT = 15
CU_JIT_FAST_COMPILE = 16
CU_JIT_GLOBAL_SYMBOL_NAMES = 17
CU_JIT_GLOBAL_SYMBOL_ADDRESSES = 18
CU_JIT_GLOBAL_SYMBOL_COUNT = 19
CU_JIT_LTO = 20
CU_JIT_FTZ = 21
CU_JIT_PREC_DIV = 22
CU_JIT_PREC_SQRT = 23
CU_JIT_FMA = 24
CU_JIT_REFERENCED_KERNEL_NAMES = 25
CU_JIT_REFERENCED_KERNEL_COUNT = 26
CU_JIT_REFERENCED_VARIABLE_NAMES = 27
CU_JIT_REFERENCED_VARIABLE_COUNT = 28
CU_JIT_OPTIMIZE_UNUSED_DEVICE_VARIABLES = 29
CU_JIT_POSITION_INDEPENDENT_CODE = 30
CU_JIT_MIN_CTA_PER_SM = 31
CU_JIT_MAX_THREADS_PER_BLOCK = 32
CU_JIT_OVERRIDE_DIRECTIVE_VALUES = 33
CU_JIT_NUM_OPTIONS = 34
ctypedef CUjit_option_enum CUjit_option
cdef enum CUjit_target_enum:
CU_TARGET_COMPUTE_30 = 30
CU_TARGET_COMPUTE_32 = 32
CU_TARGET_COMPUTE_35 = 35
CU_TARGET_COMPUTE_37 = 37
CU_TARGET_COMPUTE_50 = 50
CU_TARGET_COMPUTE_52 = 52
CU_TARGET_COMPUTE_53 = 53
CU_TARGET_COMPUTE_60 = 60
CU_TARGET_COMPUTE_61 = 61
CU_TARGET_COMPUTE_62 = 62
CU_TARGET_COMPUTE_70 = 70
CU_TARGET_COMPUTE_72 = 72
CU_TARGET_COMPUTE_75 = 75
CU_TARGET_COMPUTE_80 = 80
CU_TARGET_COMPUTE_86 = 86
CU_TARGET_COMPUTE_87 = 87
CU_TARGET_COMPUTE_89 = 89
CU_TARGET_COMPUTE_90 = 90
CU_TARGET_COMPUTE_100 = 100
CU_TARGET_COMPUTE_101 = 101
CU_TARGET_COMPUTE_103 = 103
CU_TARGET_COMPUTE_120 = 120
CU_TARGET_COMPUTE_121 = 121
CU_TARGET_COMPUTE_90A = 65626
CU_TARGET_COMPUTE_100A = 65636
CU_TARGET_COMPUTE_101A = 65637
CU_TARGET_COMPUTE_103A = 65639
CU_TARGET_COMPUTE_120A = 65656
CU_TARGET_COMPUTE_121A = 65657
CU_TARGET_COMPUTE_100F = 131172
CU_TARGET_COMPUTE_101F = 131173
CU_TARGET_COMPUTE_103F = 131175
CU_TARGET_COMPUTE_120F = 131192
CU_TARGET_COMPUTE_121F = 131193
ctypedef CUjit_target_enum CUjit_target
cdef enum CUjit_fallback_enum:
CU_PREFER_PTX = 0
CU_PREFER_BINARY = 1
ctypedef CUjit_fallback_enum CUjit_fallback
cdef enum CUjit_cacheMode_enum:
CU_JIT_CACHE_OPTION_NONE = 0
CU_JIT_CACHE_OPTION_CG = 1
CU_JIT_CACHE_OPTION_CA = 2
ctypedef CUjit_cacheMode_enum CUjit_cacheMode
cdef enum CUjitInputType_enum:
CU_JIT_INPUT_CUBIN = 0
CU_JIT_INPUT_PTX = 1
CU_JIT_INPUT_FATBINARY = 2
CU_JIT_INPUT_OBJECT = 3
CU_JIT_INPUT_LIBRARY = 4
CU_JIT_INPUT_NVVM = 5
CU_JIT_NUM_INPUT_TYPES = 6
ctypedef CUjitInputType_enum CUjitInputType
cdef struct CUlinkState_st:
pass
ctypedef CUlinkState_st* CUlinkState
cdef enum CUgraphicsRegisterFlags_enum:
CU_GRAPHICS_REGISTER_FLAGS_NONE = 0
CU_GRAPHICS_REGISTER_FLAGS_READ_ONLY = 1
CU_GRAPHICS_REGISTER_FLAGS_WRITE_DISCARD = 2
CU_GRAPHICS_REGISTER_FLAGS_SURFACE_LDST = 4
CU_GRAPHICS_REGISTER_FLAGS_TEXTURE_GATHER = 8
ctypedef CUgraphicsRegisterFlags_enum CUgraphicsRegisterFlags
cdef enum CUgraphicsMapResourceFlags_enum:
CU_GRAPHICS_MAP_RESOURCE_FLAGS_NONE = 0
CU_GRAPHICS_MAP_RESOURCE_FLAGS_READ_ONLY = 1
CU_GRAPHICS_MAP_RESOURCE_FLAGS_WRITE_DISCARD = 2
ctypedef CUgraphicsMapResourceFlags_enum CUgraphicsMapResourceFlags
cdef enum CUarray_cubemap_face_enum:
CU_CUBEMAP_FACE_POSITIVE_X = 0
CU_CUBEMAP_FACE_NEGATIVE_X = 1
CU_CUBEMAP_FACE_POSITIVE_Y = 2
CU_CUBEMAP_FACE_NEGATIVE_Y = 3
CU_CUBEMAP_FACE_POSITIVE_Z = 4
CU_CUBEMAP_FACE_NEGATIVE_Z = 5
ctypedef CUarray_cubemap_face_enum CUarray_cubemap_face
cdef enum CUlimit_enum:
CU_LIMIT_STACK_SIZE = 0
CU_LIMIT_PRINTF_FIFO_SIZE = 1
CU_LIMIT_MALLOC_HEAP_SIZE = 2
CU_LIMIT_DEV_RUNTIME_SYNC_DEPTH = 3
CU_LIMIT_DEV_RUNTIME_PENDING_LAUNCH_COUNT = 4
CU_LIMIT_MAX_L2_FETCH_GRANULARITY = 5
CU_LIMIT_PERSISTING_L2_CACHE_SIZE = 6
CU_LIMIT_SHMEM_SIZE = 7
CU_LIMIT_CIG_ENABLED = 8
CU_LIMIT_CIG_SHMEM_FALLBACK_ENABLED = 9
CU_LIMIT_MAX = 10
ctypedef CUlimit_enum CUlimit
cdef enum CUresourcetype_enum:
CU_RESOURCE_TYPE_ARRAY = 0
CU_RESOURCE_TYPE_MIPMAPPED_ARRAY = 1
CU_RESOURCE_TYPE_LINEAR = 2
CU_RESOURCE_TYPE_PITCH2D = 3
ctypedef CUresourcetype_enum CUresourcetype
ctypedef void (*CUhostFn)(void* userData)
cdef enum CUaccessProperty_enum:
CU_ACCESS_PROPERTY_NORMAL = 0
CU_ACCESS_PROPERTY_STREAMING = 1
CU_ACCESS_PROPERTY_PERSISTING = 2
ctypedef CUaccessProperty_enum CUaccessProperty
cdef struct CUaccessPolicyWindow_st:
void* base_ptr
size_t num_bytes
float hitRatio
CUaccessProperty hitProp
CUaccessProperty missProp
ctypedef CUaccessPolicyWindow_st CUaccessPolicyWindow_v1
ctypedef CUaccessPolicyWindow_v1 CUaccessPolicyWindow
cdef struct CUDA_KERNEL_NODE_PARAMS_st:
CUfunction func
unsigned int gridDimX
unsigned int gridDimY
unsigned int gridDimZ
unsigned int blockDimX
unsigned int blockDimY
unsigned int blockDimZ
unsigned int sharedMemBytes
void** kernelParams
void** extra
ctypedef CUDA_KERNEL_NODE_PARAMS_st CUDA_KERNEL_NODE_PARAMS_v1
cdef struct CUDA_KERNEL_NODE_PARAMS_v2_st:
CUfunction func
unsigned int gridDimX
unsigned int gridDimY
unsigned int gridDimZ
unsigned int blockDimX
unsigned int blockDimY
unsigned int blockDimZ
unsigned int sharedMemBytes
void** kernelParams
void** extra
CUkernel kern
CUcontext ctx
ctypedef CUDA_KERNEL_NODE_PARAMS_v2_st CUDA_KERNEL_NODE_PARAMS_v2
ctypedef CUDA_KERNEL_NODE_PARAMS_v2 CUDA_KERNEL_NODE_PARAMS
cdef struct CUDA_KERNEL_NODE_PARAMS_v3_st:
CUfunction func
unsigned int gridDimX
unsigned int gridDimY
unsigned int gridDimZ
unsigned int blockDimX
unsigned int blockDimY
unsigned int blockDimZ
unsigned int sharedMemBytes
void** kernelParams
void** extra
CUkernel kern
CUcontext ctx
ctypedef CUDA_KERNEL_NODE_PARAMS_v3_st CUDA_KERNEL_NODE_PARAMS_v3
cdef struct CUDA_MEMSET_NODE_PARAMS_st:
CUdeviceptr dst
size_t pitch
unsigned int value
unsigned int elementSize
size_t width
size_t height
ctypedef CUDA_MEMSET_NODE_PARAMS_st CUDA_MEMSET_NODE_PARAMS_v1
ctypedef CUDA_MEMSET_NODE_PARAMS_v1 CUDA_MEMSET_NODE_PARAMS
cdef struct CUDA_MEMSET_NODE_PARAMS_v2_st:
CUdeviceptr dst
size_t pitch
unsigned int value
unsigned int elementSize
size_t width
size_t height
CUcontext ctx
ctypedef CUDA_MEMSET_NODE_PARAMS_v2_st CUDA_MEMSET_NODE_PARAMS_v2
cdef struct CUDA_HOST_NODE_PARAMS_st:
CUhostFn fn
void* userData
ctypedef CUDA_HOST_NODE_PARAMS_st CUDA_HOST_NODE_PARAMS_v1
ctypedef CUDA_HOST_NODE_PARAMS_v1 CUDA_HOST_NODE_PARAMS
cdef struct CUDA_HOST_NODE_PARAMS_v2_st:
CUhostFn fn
void* userData
ctypedef CUDA_HOST_NODE_PARAMS_v2_st CUDA_HOST_NODE_PARAMS_v2
cdef enum CUgraphConditionalNodeType_enum:
CU_GRAPH_COND_TYPE_IF = 0
CU_GRAPH_COND_TYPE_WHILE = 1
CU_GRAPH_COND_TYPE_SWITCH = 2
ctypedef CUgraphConditionalNodeType_enum CUgraphConditionalNodeType
cdef struct CUDA_CONDITIONAL_NODE_PARAMS:
CUgraphConditionalHandle handle
CUgraphConditionalNodeType type
unsigned int size
CUgraph* phGraph_out
CUcontext ctx
cdef enum CUgraphNodeType_enum:
CU_GRAPH_NODE_TYPE_KERNEL = 0
CU_GRAPH_NODE_TYPE_MEMCPY = 1
CU_GRAPH_NODE_TYPE_MEMSET = 2
CU_GRAPH_NODE_TYPE_HOST = 3
CU_GRAPH_NODE_TYPE_GRAPH = 4
CU_GRAPH_NODE_TYPE_EMPTY = 5
CU_GRAPH_NODE_TYPE_WAIT_EVENT = 6
CU_GRAPH_NODE_TYPE_EVENT_RECORD = 7
CU_GRAPH_NODE_TYPE_EXT_SEMAS_SIGNAL = 8
CU_GRAPH_NODE_TYPE_EXT_SEMAS_WAIT = 9
CU_GRAPH_NODE_TYPE_MEM_ALLOC = 10
CU_GRAPH_NODE_TYPE_MEM_FREE = 11
CU_GRAPH_NODE_TYPE_BATCH_MEM_OP = 12
CU_GRAPH_NODE_TYPE_CONDITIONAL = 13
ctypedef CUgraphNodeType_enum CUgraphNodeType
cdef enum CUgraphDependencyType_enum:
CU_GRAPH_DEPENDENCY_TYPE_DEFAULT = 0
CU_GRAPH_DEPENDENCY_TYPE_PROGRAMMATIC = 1
ctypedef CUgraphDependencyType_enum CUgraphDependencyType
cdef struct CUgraphEdgeData_st:
unsigned char from_port
unsigned char to_port
unsigned char type
unsigned char reserved[5]
ctypedef CUgraphEdgeData_st CUgraphEdgeData
cdef enum CUgraphInstantiateResult_enum:
CUDA_GRAPH_INSTANTIATE_SUCCESS = 0
CUDA_GRAPH_INSTANTIATE_ERROR = 1
CUDA_GRAPH_INSTANTIATE_INVALID_STRUCTURE = 2
CUDA_GRAPH_INSTANTIATE_NODE_OPERATION_NOT_SUPPORTED = 3
CUDA_GRAPH_INSTANTIATE_MULTIPLE_CTXS_NOT_SUPPORTED = 4
CUDA_GRAPH_INSTANTIATE_CONDITIONAL_HANDLE_UNUSED = 5
ctypedef CUgraphInstantiateResult_enum CUgraphInstantiateResult
cdef struct CUDA_GRAPH_INSTANTIATE_PARAMS_st:
cuuint64_t flags
CUstream hUploadStream
CUgraphNode hErrNode_out
CUgraphInstantiateResult result_out
ctypedef CUDA_GRAPH_INSTANTIATE_PARAMS_st CUDA_GRAPH_INSTANTIATE_PARAMS
cdef enum CUsynchronizationPolicy_enum:
CU_SYNC_POLICY_AUTO = 1
CU_SYNC_POLICY_SPIN = 2
CU_SYNC_POLICY_YIELD = 3
CU_SYNC_POLICY_BLOCKING_SYNC = 4
ctypedef CUsynchronizationPolicy_enum CUsynchronizationPolicy
cdef enum CUclusterSchedulingPolicy_enum:
CU_CLUSTER_SCHEDULING_POLICY_DEFAULT = 0
CU_CLUSTER_SCHEDULING_POLICY_SPREAD = 1
CU_CLUSTER_SCHEDULING_POLICY_LOAD_BALANCING = 2
ctypedef CUclusterSchedulingPolicy_enum CUclusterSchedulingPolicy
cdef enum CUlaunchMemSyncDomain_enum:
CU_LAUNCH_MEM_SYNC_DOMAIN_DEFAULT = 0
CU_LAUNCH_MEM_SYNC_DOMAIN_REMOTE = 1
ctypedef CUlaunchMemSyncDomain_enum CUlaunchMemSyncDomain
cdef struct CUlaunchMemSyncDomainMap_st:
unsigned char default_
unsigned char remote
ctypedef CUlaunchMemSyncDomainMap_st CUlaunchMemSyncDomainMap
cdef enum CUlaunchAttributeID_enum:
CU_LAUNCH_ATTRIBUTE_IGNORE = 0
CU_LAUNCH_ATTRIBUTE_ACCESS_POLICY_WINDOW = 1
CU_LAUNCH_ATTRIBUTE_COOPERATIVE = 2
CU_LAUNCH_ATTRIBUTE_SYNCHRONIZATION_POLICY = 3
CU_LAUNCH_ATTRIBUTE_CLUSTER_DIMENSION = 4
CU_LAUNCH_ATTRIBUTE_CLUSTER_SCHEDULING_POLICY_PREFERENCE = 5
CU_LAUNCH_ATTRIBUTE_PROGRAMMATIC_STREAM_SERIALIZATION = 6
CU_LAUNCH_ATTRIBUTE_PROGRAMMATIC_EVENT = 7
CU_LAUNCH_ATTRIBUTE_PRIORITY = 8
CU_LAUNCH_ATTRIBUTE_MEM_SYNC_DOMAIN_MAP = 9
CU_LAUNCH_ATTRIBUTE_MEM_SYNC_DOMAIN = 10
CU_LAUNCH_ATTRIBUTE_PREFERRED_CLUSTER_DIMENSION = 11
CU_LAUNCH_ATTRIBUTE_LAUNCH_COMPLETION_EVENT = 12
CU_LAUNCH_ATTRIBUTE_DEVICE_UPDATABLE_KERNEL_NODE = 13
CU_LAUNCH_ATTRIBUTE_PREFERRED_SHARED_MEMORY_CARVEOUT = 14
ctypedef CUlaunchAttributeID_enum CUlaunchAttributeID
cdef struct anon_struct1:
unsigned int x
unsigned int y
unsigned int z
cdef struct anon_struct2:
CUevent event
int flags
int triggerAtBlockStart
cdef struct anon_struct3:
CUevent event
int flags
cdef struct anon_struct4:
unsigned int x
unsigned int y
unsigned int z
cdef struct anon_struct5:
int deviceUpdatable
CUgraphDeviceNode devNode
cdef union CUlaunchAttributeValue_union:
char pad[64]
CUaccessPolicyWindow accessPolicyWindow
int cooperative
CUsynchronizationPolicy syncPolicy
anon_struct1 clusterDim
CUclusterSchedulingPolicy clusterSchedulingPolicyPreference
int programmaticStreamSerializationAllowed
anon_struct2 programmaticEvent
anon_struct3 launchCompletionEvent
int priority
CUlaunchMemSyncDomainMap memSyncDomainMap
CUlaunchMemSyncDomain memSyncDomain
anon_struct4 preferredClusterDim
anon_struct5 deviceUpdatableKernelNode
unsigned int sharedMemCarveout
ctypedef CUlaunchAttributeValue_union CUlaunchAttributeValue
cdef struct CUlaunchAttribute_st:
CUlaunchAttributeID id
CUlaunchAttributeValue value
ctypedef CUlaunchAttribute_st CUlaunchAttribute
cdef struct CUlaunchConfig_st:
unsigned int gridDimX
unsigned int gridDimY
unsigned int gridDimZ
unsigned int blockDimX
unsigned int blockDimY
unsigned int blockDimZ
unsigned int sharedMemBytes
CUstream hStream
CUlaunchAttribute* attrs
unsigned int numAttrs
ctypedef CUlaunchConfig_st CUlaunchConfig
ctypedef CUlaunchAttributeID CUkernelNodeAttrID
ctypedef CUlaunchAttributeValue CUkernelNodeAttrValue_v1
ctypedef CUkernelNodeAttrValue_v1 CUkernelNodeAttrValue
cdef enum CUstreamCaptureStatus_enum:
CU_STREAM_CAPTURE_STATUS_NONE = 0
CU_STREAM_CAPTURE_STATUS_ACTIVE = 1
CU_STREAM_CAPTURE_STATUS_INVALIDATED = 2
ctypedef CUstreamCaptureStatus_enum CUstreamCaptureStatus
cdef enum CUstreamCaptureMode_enum:
CU_STREAM_CAPTURE_MODE_GLOBAL = 0
CU_STREAM_CAPTURE_MODE_THREAD_LOCAL = 1
CU_STREAM_CAPTURE_MODE_RELAXED = 2
ctypedef CUstreamCaptureMode_enum CUstreamCaptureMode
ctypedef CUlaunchAttributeID CUstreamAttrID
ctypedef CUlaunchAttributeValue CUstreamAttrValue_v1
ctypedef CUstreamAttrValue_v1 CUstreamAttrValue
cdef enum CUdriverProcAddress_flags_enum:
CU_GET_PROC_ADDRESS_DEFAULT = 0
CU_GET_PROC_ADDRESS_LEGACY_STREAM = 1
CU_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM = 2
ctypedef CUdriverProcAddress_flags_enum CUdriverProcAddress_flags
cdef enum CUdriverProcAddressQueryResult_enum:
CU_GET_PROC_ADDRESS_SUCCESS = 0
CU_GET_PROC_ADDRESS_SYMBOL_NOT_FOUND = 1
CU_GET_PROC_ADDRESS_VERSION_NOT_SUFFICIENT = 2
ctypedef CUdriverProcAddressQueryResult_enum CUdriverProcAddressQueryResult
cdef enum CUexecAffinityType_enum:
CU_EXEC_AFFINITY_TYPE_SM_COUNT = 0
CU_EXEC_AFFINITY_TYPE_MAX = 1
ctypedef CUexecAffinityType_enum CUexecAffinityType
cdef struct CUexecAffinitySmCount_st:
unsigned int val
ctypedef CUexecAffinitySmCount_st CUexecAffinitySmCount_v1
ctypedef CUexecAffinitySmCount_v1 CUexecAffinitySmCount
cdef union anon_union3:
CUexecAffinitySmCount smCount
cdef struct CUexecAffinityParam_st:
CUexecAffinityType type
anon_union3 param
ctypedef CUexecAffinityParam_st CUexecAffinityParam_v1
ctypedef CUexecAffinityParam_v1 CUexecAffinityParam
cdef enum CUcigDataType_enum:
CIG_DATA_TYPE_D3D12_COMMAND_QUEUE = 1
CIG_DATA_TYPE_NV_BLOB = 2
ctypedef CUcigDataType_enum CUcigDataType
cdef struct CUctxCigParam_st:
CUcigDataType sharedDataType
void* sharedData
ctypedef CUctxCigParam_st CUctxCigParam
cdef struct CUctxCreateParams_st:
CUexecAffinityParam* execAffinityParams
int numExecAffinityParams
CUctxCigParam* cigParams
ctypedef CUctxCreateParams_st CUctxCreateParams
cdef enum CUlibraryOption_enum:
CU_LIBRARY_HOST_UNIVERSAL_FUNCTION_AND_DATA_TABLE = 0
CU_LIBRARY_BINARY_IS_PRESERVED = 1
CU_LIBRARY_NUM_OPTIONS = 2
ctypedef CUlibraryOption_enum CUlibraryOption
cdef struct CUlibraryHostUniversalFunctionAndDataTable_st:
void* functionTable
size_t functionWindowSize
void* dataTable
size_t dataWindowSize
ctypedef CUlibraryHostUniversalFunctionAndDataTable_st CUlibraryHostUniversalFunctionAndDataTable
cdef enum cudaError_enum:
CUDA_SUCCESS = 0
CUDA_ERROR_INVALID_VALUE = 1
CUDA_ERROR_OUT_OF_MEMORY = 2
CUDA_ERROR_NOT_INITIALIZED = 3
CUDA_ERROR_DEINITIALIZED = 4
CUDA_ERROR_PROFILER_DISABLED = 5
CUDA_ERROR_PROFILER_NOT_INITIALIZED = 6
CUDA_ERROR_PROFILER_ALREADY_STARTED = 7
CUDA_ERROR_PROFILER_ALREADY_STOPPED = 8
CUDA_ERROR_STUB_LIBRARY = 34
CUDA_ERROR_DEVICE_UNAVAILABLE = 46
CUDA_ERROR_NO_DEVICE = 100
CUDA_ERROR_INVALID_DEVICE = 101
CUDA_ERROR_DEVICE_NOT_LICENSED = 102
CUDA_ERROR_INVALID_IMAGE = 200
CUDA_ERROR_INVALID_CONTEXT = 201
CUDA_ERROR_CONTEXT_ALREADY_CURRENT = 202
CUDA_ERROR_MAP_FAILED = 205
CUDA_ERROR_UNMAP_FAILED = 206
CUDA_ERROR_ARRAY_IS_MAPPED = 207
CUDA_ERROR_ALREADY_MAPPED = 208
CUDA_ERROR_NO_BINARY_FOR_GPU = 209
CUDA_ERROR_ALREADY_ACQUIRED = 210
CUDA_ERROR_NOT_MAPPED = 211
CUDA_ERROR_NOT_MAPPED_AS_ARRAY = 212
CUDA_ERROR_NOT_MAPPED_AS_POINTER = 213
CUDA_ERROR_ECC_UNCORRECTABLE = 214
CUDA_ERROR_UNSUPPORTED_LIMIT = 215
CUDA_ERROR_CONTEXT_ALREADY_IN_USE = 216
CUDA_ERROR_PEER_ACCESS_UNSUPPORTED = 217
CUDA_ERROR_INVALID_PTX = 218
CUDA_ERROR_INVALID_GRAPHICS_CONTEXT = 219
CUDA_ERROR_NVLINK_UNCORRECTABLE = 220
CUDA_ERROR_JIT_COMPILER_NOT_FOUND = 221
CUDA_ERROR_UNSUPPORTED_PTX_VERSION = 222
CUDA_ERROR_JIT_COMPILATION_DISABLED = 223
CUDA_ERROR_UNSUPPORTED_EXEC_AFFINITY = 224
CUDA_ERROR_UNSUPPORTED_DEVSIDE_SYNC = 225
CUDA_ERROR_CONTAINED = 226
CUDA_ERROR_INVALID_SOURCE = 300
CUDA_ERROR_FILE_NOT_FOUND = 301
CUDA_ERROR_SHARED_OBJECT_SYMBOL_NOT_FOUND = 302
CUDA_ERROR_SHARED_OBJECT_INIT_FAILED = 303
CUDA_ERROR_OPERATING_SYSTEM = 304
CUDA_ERROR_INVALID_HANDLE = 400
CUDA_ERROR_ILLEGAL_STATE = 401
CUDA_ERROR_LOSSY_QUERY = 402
CUDA_ERROR_NOT_FOUND = 500
CUDA_ERROR_NOT_READY = 600
CUDA_ERROR_ILLEGAL_ADDRESS = 700
CUDA_ERROR_LAUNCH_OUT_OF_RESOURCES = 701
CUDA_ERROR_LAUNCH_TIMEOUT = 702
CUDA_ERROR_LAUNCH_INCOMPATIBLE_TEXTURING = 703
CUDA_ERROR_PEER_ACCESS_ALREADY_ENABLED = 704
CUDA_ERROR_PEER_ACCESS_NOT_ENABLED = 705
CUDA_ERROR_PRIMARY_CONTEXT_ACTIVE = 708
CUDA_ERROR_CONTEXT_IS_DESTROYED = 709
CUDA_ERROR_ASSERT = 710
CUDA_ERROR_TOO_MANY_PEERS = 711
CUDA_ERROR_HOST_MEMORY_ALREADY_REGISTERED = 712
CUDA_ERROR_HOST_MEMORY_NOT_REGISTERED = 713
CUDA_ERROR_HARDWARE_STACK_ERROR = 714
CUDA_ERROR_ILLEGAL_INSTRUCTION = 715
CUDA_ERROR_MISALIGNED_ADDRESS = 716
CUDA_ERROR_INVALID_ADDRESS_SPACE = 717
CUDA_ERROR_INVALID_PC = 718
CUDA_ERROR_LAUNCH_FAILED = 719
CUDA_ERROR_COOPERATIVE_LAUNCH_TOO_LARGE = 720
CUDA_ERROR_TENSOR_MEMORY_LEAK = 721
CUDA_ERROR_NOT_PERMITTED = 800
CUDA_ERROR_NOT_SUPPORTED = 801
CUDA_ERROR_SYSTEM_NOT_READY = 802
CUDA_ERROR_SYSTEM_DRIVER_MISMATCH = 803
CUDA_ERROR_COMPAT_NOT_SUPPORTED_ON_DEVICE = 804
CUDA_ERROR_MPS_CONNECTION_FAILED = 805
CUDA_ERROR_MPS_RPC_FAILURE = 806
CUDA_ERROR_MPS_SERVER_NOT_READY = 807
CUDA_ERROR_MPS_MAX_CLIENTS_REACHED = 808
CUDA_ERROR_MPS_MAX_CONNECTIONS_REACHED = 809
CUDA_ERROR_MPS_CLIENT_TERMINATED = 810
CUDA_ERROR_CDP_NOT_SUPPORTED = 811
CUDA_ERROR_CDP_VERSION_MISMATCH = 812
CUDA_ERROR_STREAM_CAPTURE_UNSUPPORTED = 900
CUDA_ERROR_STREAM_CAPTURE_INVALIDATED = 901
CUDA_ERROR_STREAM_CAPTURE_MERGE = 902
CUDA_ERROR_STREAM_CAPTURE_UNMATCHED = 903
CUDA_ERROR_STREAM_CAPTURE_UNJOINED = 904
CUDA_ERROR_STREAM_CAPTURE_ISOLATION = 905
CUDA_ERROR_STREAM_CAPTURE_IMPLICIT = 906
CUDA_ERROR_CAPTURED_EVENT = 907
CUDA_ERROR_STREAM_CAPTURE_WRONG_THREAD = 908
CUDA_ERROR_TIMEOUT = 909
CUDA_ERROR_GRAPH_EXEC_UPDATE_FAILURE = 910
CUDA_ERROR_EXTERNAL_DEVICE = 911
CUDA_ERROR_INVALID_CLUSTER_SIZE = 912
CUDA_ERROR_FUNCTION_NOT_LOADED = 913
CUDA_ERROR_INVALID_RESOURCE_TYPE = 914
CUDA_ERROR_INVALID_RESOURCE_CONFIGURATION = 915
CUDA_ERROR_KEY_ROTATION = 916
CUDA_ERROR_UNKNOWN = 999
ctypedef cudaError_enum CUresult
cdef enum CUdevice_P2PAttribute_enum:
CU_DEVICE_P2P_ATTRIBUTE_PERFORMANCE_RANK = 1
CU_DEVICE_P2P_ATTRIBUTE_ACCESS_SUPPORTED = 2
CU_DEVICE_P2P_ATTRIBUTE_NATIVE_ATOMIC_SUPPORTED = 3
CU_DEVICE_P2P_ATTRIBUTE_ACCESS_ACCESS_SUPPORTED = 4
CU_DEVICE_P2P_ATTRIBUTE_CUDA_ARRAY_ACCESS_SUPPORTED = 4
ctypedef CUdevice_P2PAttribute_enum CUdevice_P2PAttribute
ctypedef void (*CUstreamCallback)(CUstream hStream, CUresult status, void* userData)
ctypedef size_t (*CUoccupancyB2DSize)(int blockSize)
cdef struct CUDA_MEMCPY2D_st:
size_t srcXInBytes
size_t srcY
CUmemorytype srcMemoryType
const void* srcHost
CUdeviceptr srcDevice
CUarray srcArray
size_t srcPitch
size_t dstXInBytes
size_t dstY
CUmemorytype dstMemoryType
void* dstHost
CUdeviceptr dstDevice
CUarray dstArray
size_t dstPitch
size_t WidthInBytes
size_t Height
ctypedef CUDA_MEMCPY2D_st CUDA_MEMCPY2D_v2
ctypedef CUDA_MEMCPY2D_v2 CUDA_MEMCPY2D
cdef struct CUDA_MEMCPY3D_st:
size_t srcXInBytes
size_t srcY
size_t srcZ
size_t srcLOD
CUmemorytype srcMemoryType
const void* srcHost
CUdeviceptr srcDevice
CUarray srcArray
void* reserved0
size_t srcPitch
size_t srcHeight
size_t dstXInBytes
size_t dstY
size_t dstZ
size_t dstLOD
CUmemorytype dstMemoryType
void* dstHost
CUdeviceptr dstDevice
CUarray dstArray
void* reserved1
size_t dstPitch
size_t dstHeight
size_t WidthInBytes
size_t Height
size_t Depth
ctypedef CUDA_MEMCPY3D_st CUDA_MEMCPY3D_v2
ctypedef CUDA_MEMCPY3D_v2 CUDA_MEMCPY3D
cdef struct CUDA_MEMCPY3D_PEER_st:
size_t srcXInBytes
size_t srcY
size_t srcZ
size_t srcLOD
CUmemorytype srcMemoryType
const void* srcHost
CUdeviceptr srcDevice
CUarray srcArray
CUcontext srcContext
size_t srcPitch
size_t srcHeight
size_t dstXInBytes
size_t dstY
size_t dstZ
size_t dstLOD
CUmemorytype dstMemoryType
void* dstHost
CUdeviceptr dstDevice
CUarray dstArray
CUcontext dstContext
size_t dstPitch
size_t dstHeight
size_t WidthInBytes
size_t Height
size_t Depth
ctypedef CUDA_MEMCPY3D_PEER_st CUDA_MEMCPY3D_PEER_v1
ctypedef CUDA_MEMCPY3D_PEER_v1 CUDA_MEMCPY3D_PEER
cdef struct CUDA_MEMCPY_NODE_PARAMS_st:
int flags
int reserved
CUcontext copyCtx
CUDA_MEMCPY3D copyParams
ctypedef CUDA_MEMCPY_NODE_PARAMS_st CUDA_MEMCPY_NODE_PARAMS
cdef struct CUDA_ARRAY_DESCRIPTOR_st:
size_t Width
size_t Height
CUarray_format Format
unsigned int NumChannels
ctypedef CUDA_ARRAY_DESCRIPTOR_st CUDA_ARRAY_DESCRIPTOR_v2
ctypedef CUDA_ARRAY_DESCRIPTOR_v2 CUDA_ARRAY_DESCRIPTOR
cdef struct CUDA_ARRAY3D_DESCRIPTOR_st:
size_t Width
size_t Height
size_t Depth
CUarray_format Format
unsigned int NumChannels
unsigned int Flags
ctypedef CUDA_ARRAY3D_DESCRIPTOR_st CUDA_ARRAY3D_DESCRIPTOR_v2
ctypedef CUDA_ARRAY3D_DESCRIPTOR_v2 CUDA_ARRAY3D_DESCRIPTOR
cdef struct anon_struct6:
unsigned int width
unsigned int height
unsigned int depth
cdef struct CUDA_ARRAY_SPARSE_PROPERTIES_st:
anon_struct6 tileExtent
unsigned int miptailFirstLevel
unsigned long long miptailSize
unsigned int flags
unsigned int reserved[4]
ctypedef CUDA_ARRAY_SPARSE_PROPERTIES_st CUDA_ARRAY_SPARSE_PROPERTIES_v1
ctypedef CUDA_ARRAY_SPARSE_PROPERTIES_v1 CUDA_ARRAY_SPARSE_PROPERTIES
cdef struct CUDA_ARRAY_MEMORY_REQUIREMENTS_st:
size_t size
size_t alignment
unsigned int reserved[4]
ctypedef CUDA_ARRAY_MEMORY_REQUIREMENTS_st CUDA_ARRAY_MEMORY_REQUIREMENTS_v1
ctypedef CUDA_ARRAY_MEMORY_REQUIREMENTS_v1 CUDA_ARRAY_MEMORY_REQUIREMENTS
cdef struct anon_struct7:
CUarray hArray
cdef struct anon_struct8:
CUmipmappedArray hMipmappedArray
cdef struct anon_struct9:
CUdeviceptr devPtr
CUarray_format format
unsigned int numChannels
size_t sizeInBytes
cdef struct anon_struct10:
CUdeviceptr devPtr
CUarray_format format
unsigned int numChannels
size_t width
size_t height
size_t pitchInBytes
cdef struct anon_struct11:
int reserved[32]
cdef union anon_union4:
anon_struct7 array
anon_struct8 mipmap
anon_struct9 linear
anon_struct10 pitch2D
anon_struct11 reserved
cdef struct CUDA_RESOURCE_DESC_st:
CUresourcetype resType
anon_union4 res
unsigned int flags
ctypedef CUDA_RESOURCE_DESC_st CUDA_RESOURCE_DESC_v1
ctypedef CUDA_RESOURCE_DESC_v1 CUDA_RESOURCE_DESC
cdef struct CUDA_TEXTURE_DESC_st:
CUaddress_mode addressMode[3]
CUfilter_mode filterMode
unsigned int flags
unsigned int maxAnisotropy
CUfilter_mode mipmapFilterMode
float mipmapLevelBias
float minMipmapLevelClamp
float maxMipmapLevelClamp
float borderColor[4]
int reserved[12]
ctypedef CUDA_TEXTURE_DESC_st CUDA_TEXTURE_DESC_v1
ctypedef CUDA_TEXTURE_DESC_v1 CUDA_TEXTURE_DESC
cdef enum CUresourceViewFormat_enum:
CU_RES_VIEW_FORMAT_NONE = 0
CU_RES_VIEW_FORMAT_UINT_1X8 = 1
CU_RES_VIEW_FORMAT_UINT_2X8 = 2
CU_RES_VIEW_FORMAT_UINT_4X8 = 3
CU_RES_VIEW_FORMAT_SINT_1X8 = 4
CU_RES_VIEW_FORMAT_SINT_2X8 = 5
CU_RES_VIEW_FORMAT_SINT_4X8 = 6
CU_RES_VIEW_FORMAT_UINT_1X16 = 7
CU_RES_VIEW_FORMAT_UINT_2X16 = 8
CU_RES_VIEW_FORMAT_UINT_4X16 = 9
CU_RES_VIEW_FORMAT_SINT_1X16 = 10
CU_RES_VIEW_FORMAT_SINT_2X16 = 11
CU_RES_VIEW_FORMAT_SINT_4X16 = 12
CU_RES_VIEW_FORMAT_UINT_1X32 = 13
CU_RES_VIEW_FORMAT_UINT_2X32 = 14
CU_RES_VIEW_FORMAT_UINT_4X32 = 15
CU_RES_VIEW_FORMAT_SINT_1X32 = 16
CU_RES_VIEW_FORMAT_SINT_2X32 = 17
CU_RES_VIEW_FORMAT_SINT_4X32 = 18
CU_RES_VIEW_FORMAT_FLOAT_1X16 = 19
CU_RES_VIEW_FORMAT_FLOAT_2X16 = 20
CU_RES_VIEW_FORMAT_FLOAT_4X16 = 21
CU_RES_VIEW_FORMAT_FLOAT_1X32 = 22
CU_RES_VIEW_FORMAT_FLOAT_2X32 = 23
CU_RES_VIEW_FORMAT_FLOAT_4X32 = 24
CU_RES_VIEW_FORMAT_UNSIGNED_BC1 = 25
CU_RES_VIEW_FORMAT_UNSIGNED_BC2 = 26
CU_RES_VIEW_FORMAT_UNSIGNED_BC3 = 27
CU_RES_VIEW_FORMAT_UNSIGNED_BC4 = 28
CU_RES_VIEW_FORMAT_SIGNED_BC4 = 29
CU_RES_VIEW_FORMAT_UNSIGNED_BC5 = 30
CU_RES_VIEW_FORMAT_SIGNED_BC5 = 31
CU_RES_VIEW_FORMAT_UNSIGNED_BC6H = 32
CU_RES_VIEW_FORMAT_SIGNED_BC6H = 33
CU_RES_VIEW_FORMAT_UNSIGNED_BC7 = 34
ctypedef CUresourceViewFormat_enum CUresourceViewFormat
cdef struct CUDA_RESOURCE_VIEW_DESC_st:
CUresourceViewFormat format
size_t width
size_t height
size_t depth
unsigned int firstMipmapLevel
unsigned int lastMipmapLevel
unsigned int firstLayer
unsigned int lastLayer
unsigned int reserved[16]
ctypedef CUDA_RESOURCE_VIEW_DESC_st CUDA_RESOURCE_VIEW_DESC_v1
ctypedef CUDA_RESOURCE_VIEW_DESC_v1 CUDA_RESOURCE_VIEW_DESC
cdef struct CUtensorMap_st:
cuuint64_t opaque[16]
ctypedef CUtensorMap_st CUtensorMap
cdef enum CUtensorMapDataType_enum:
CU_TENSOR_MAP_DATA_TYPE_UINT8 = 0
CU_TENSOR_MAP_DATA_TYPE_UINT16 = 1
CU_TENSOR_MAP_DATA_TYPE_UINT32 = 2
CU_TENSOR_MAP_DATA_TYPE_INT32 = 3
CU_TENSOR_MAP_DATA_TYPE_UINT64 = 4
CU_TENSOR_MAP_DATA_TYPE_INT64 = 5
CU_TENSOR_MAP_DATA_TYPE_FLOAT16 = 6
CU_TENSOR_MAP_DATA_TYPE_FLOAT32 = 7
CU_TENSOR_MAP_DATA_TYPE_FLOAT64 = 8
CU_TENSOR_MAP_DATA_TYPE_BFLOAT16 = 9
CU_TENSOR_MAP_DATA_TYPE_FLOAT32_FTZ = 10
CU_TENSOR_MAP_DATA_TYPE_TFLOAT32 = 11
CU_TENSOR_MAP_DATA_TYPE_TFLOAT32_FTZ = 12
CU_TENSOR_MAP_DATA_TYPE_16U4_ALIGN8B = 13
CU_TENSOR_MAP_DATA_TYPE_16U4_ALIGN16B = 14
CU_TENSOR_MAP_DATA_TYPE_16U6_ALIGN16B = 15
ctypedef CUtensorMapDataType_enum CUtensorMapDataType
cdef enum CUtensorMapInterleave_enum:
CU_TENSOR_MAP_INTERLEAVE_NONE = 0
CU_TENSOR_MAP_INTERLEAVE_16B = 1
CU_TENSOR_MAP_INTERLEAVE_32B = 2
ctypedef CUtensorMapInterleave_enum CUtensorMapInterleave
cdef enum CUtensorMapSwizzle_enum:
CU_TENSOR_MAP_SWIZZLE_NONE = 0
CU_TENSOR_MAP_SWIZZLE_32B = 1
CU_TENSOR_MAP_SWIZZLE_64B = 2
CU_TENSOR_MAP_SWIZZLE_128B = 3
CU_TENSOR_MAP_SWIZZLE_128B_ATOM_32B = 4
CU_TENSOR_MAP_SWIZZLE_128B_ATOM_32B_FLIP_8B = 5
CU_TENSOR_MAP_SWIZZLE_128B_ATOM_64B = 6
ctypedef CUtensorMapSwizzle_enum CUtensorMapSwizzle
cdef enum CUtensorMapL2promotion_enum:
CU_TENSOR_MAP_L2_PROMOTION_NONE = 0
CU_TENSOR_MAP_L2_PROMOTION_L2_64B = 1
CU_TENSOR_MAP_L2_PROMOTION_L2_128B = 2
CU_TENSOR_MAP_L2_PROMOTION_L2_256B = 3
ctypedef CUtensorMapL2promotion_enum CUtensorMapL2promotion
cdef enum CUtensorMapFloatOOBfill_enum:
CU_TENSOR_MAP_FLOAT_OOB_FILL_NONE = 0
CU_TENSOR_MAP_FLOAT_OOB_FILL_NAN_REQUEST_ZERO_FMA = 1
ctypedef CUtensorMapFloatOOBfill_enum CUtensorMapFloatOOBfill
cdef enum CUtensorMapIm2ColWideMode_enum:
CU_TENSOR_MAP_IM2COL_WIDE_MODE_W = 0
CU_TENSOR_MAP_IM2COL_WIDE_MODE_W128 = 1
ctypedef CUtensorMapIm2ColWideMode_enum CUtensorMapIm2ColWideMode
cdef struct CUDA_POINTER_ATTRIBUTE_P2P_TOKENS_st:
unsigned long long p2pToken
unsigned int vaSpaceToken
ctypedef CUDA_POINTER_ATTRIBUTE_P2P_TOKENS_st CUDA_POINTER_ATTRIBUTE_P2P_TOKENS_v1
ctypedef CUDA_POINTER_ATTRIBUTE_P2P_TOKENS_v1 CUDA_POINTER_ATTRIBUTE_P2P_TOKENS
cdef enum CUDA_POINTER_ATTRIBUTE_ACCESS_FLAGS_enum:
CU_POINTER_ATTRIBUTE_ACCESS_FLAG_NONE = 0
CU_POINTER_ATTRIBUTE_ACCESS_FLAG_READ = 1
CU_POINTER_ATTRIBUTE_ACCESS_FLAG_READWRITE = 3
ctypedef CUDA_POINTER_ATTRIBUTE_ACCESS_FLAGS_enum CUDA_POINTER_ATTRIBUTE_ACCESS_FLAGS
cdef struct CUDA_LAUNCH_PARAMS_st:
CUfunction function
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
ctypedef CUDA_LAUNCH_PARAMS_st CUDA_LAUNCH_PARAMS_v1
ctypedef CUDA_LAUNCH_PARAMS_v1 CUDA_LAUNCH_PARAMS
cdef enum CUexternalMemoryHandleType_enum:
CU_EXTERNAL_MEMORY_HANDLE_TYPE_OPAQUE_FD = 1
CU_EXTERNAL_MEMORY_HANDLE_TYPE_OPAQUE_WIN32 = 2
CU_EXTERNAL_MEMORY_HANDLE_TYPE_OPAQUE_WIN32_KMT = 3
CU_EXTERNAL_MEMORY_HANDLE_TYPE_D3D12_HEAP = 4
CU_EXTERNAL_MEMORY_HANDLE_TYPE_D3D12_RESOURCE = 5
CU_EXTERNAL_MEMORY_HANDLE_TYPE_D3D11_RESOURCE = 6
CU_EXTERNAL_MEMORY_HANDLE_TYPE_D3D11_RESOURCE_KMT = 7
CU_EXTERNAL_MEMORY_HANDLE_TYPE_NVSCIBUF = 8
ctypedef CUexternalMemoryHandleType_enum CUexternalMemoryHandleType
cdef struct anon_struct12:
void* handle
const void* name
cdef union anon_union5:
int fd
anon_struct12 win32
const void* nvSciBufObject
cdef struct CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st:
CUexternalMemoryHandleType type
anon_union5 handle
unsigned long long size
unsigned int flags
unsigned int reserved[16]
ctypedef CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st CUDA_EXTERNAL_MEMORY_HANDLE_DESC_v1
ctypedef CUDA_EXTERNAL_MEMORY_HANDLE_DESC_v1 CUDA_EXTERNAL_MEMORY_HANDLE_DESC
cdef struct CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st:
unsigned long long offset
unsigned long long size
unsigned int flags
unsigned int reserved[16]
ctypedef CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st CUDA_EXTERNAL_MEMORY_BUFFER_DESC_v1
ctypedef CUDA_EXTERNAL_MEMORY_BUFFER_DESC_v1 CUDA_EXTERNAL_MEMORY_BUFFER_DESC
cdef struct CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st:
unsigned long long offset
CUDA_ARRAY3D_DESCRIPTOR arrayDesc
unsigned int numLevels
unsigned int reserved[16]
ctypedef CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_v1
ctypedef CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_v1 CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC
cdef enum CUexternalSemaphoreHandleType_enum:
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_OPAQUE_FD = 1
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_OPAQUE_WIN32 = 2
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_OPAQUE_WIN32_KMT = 3
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_D3D12_FENCE = 4
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_D3D11_FENCE = 5
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_NVSCISYNC = 6
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_D3D11_KEYED_MUTEX = 7
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_D3D11_KEYED_MUTEX_KMT = 8
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_TIMELINE_SEMAPHORE_FD = 9
CU_EXTERNAL_SEMAPHORE_HANDLE_TYPE_TIMELINE_SEMAPHORE_WIN32 = 10
ctypedef CUexternalSemaphoreHandleType_enum CUexternalSemaphoreHandleType
cdef struct anon_struct13:
void* handle
const void* name
cdef union anon_union6:
int fd
anon_struct13 win32
const void* nvSciSyncObj
cdef struct CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st:
CUexternalSemaphoreHandleType type
anon_union6 handle
unsigned int flags
unsigned int reserved[16]
ctypedef CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_v1
ctypedef CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_v1 CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC
cdef struct anon_struct14:
unsigned long long value
cdef union anon_union7:
void* fence
unsigned long long reserved
cdef struct anon_struct15:
unsigned long long key
cdef struct anon_struct16:
anon_struct14 fence
anon_union7 nvSciSync
anon_struct15 keyedMutex
unsigned int reserved[12]
cdef struct CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st:
anon_struct16 params
unsigned int flags
unsigned int reserved[16]
ctypedef CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_v1
ctypedef CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_v1 CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS
cdef struct anon_struct17:
unsigned long long value
cdef union anon_union8:
void* fence
unsigned long long reserved
cdef struct anon_struct18:
unsigned long long key
unsigned int timeoutMs
cdef struct anon_struct19:
anon_struct17 fence
anon_union8 nvSciSync
anon_struct18 keyedMutex
unsigned int reserved[10]
cdef struct CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st:
anon_struct19 params
unsigned int flags
unsigned int reserved[16]
ctypedef CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_v1
ctypedef CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_v1 CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS
cdef struct CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st:
CUexternalSemaphore* extSemArray
const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* paramsArray
unsigned int numExtSems
ctypedef CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v1
ctypedef CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v1 CUDA_EXT_SEM_SIGNAL_NODE_PARAMS
cdef struct CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st:
CUexternalSemaphore* extSemArray
const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* paramsArray
unsigned int numExtSems
ctypedef CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2
cdef struct CUDA_EXT_SEM_WAIT_NODE_PARAMS_st:
CUexternalSemaphore* extSemArray
const CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* paramsArray
unsigned int numExtSems
ctypedef CUDA_EXT_SEM_WAIT_NODE_PARAMS_st CUDA_EXT_SEM_WAIT_NODE_PARAMS_v1
ctypedef CUDA_EXT_SEM_WAIT_NODE_PARAMS_v1 CUDA_EXT_SEM_WAIT_NODE_PARAMS
cdef struct CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st:
CUexternalSemaphore* extSemArray
const CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* paramsArray
unsigned int numExtSems
ctypedef CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2
ctypedef unsigned long long CUmemGenericAllocationHandle_v1
ctypedef CUmemGenericAllocationHandle_v1 CUmemGenericAllocationHandle
cdef enum CUmemAllocationHandleType_enum:
CU_MEM_HANDLE_TYPE_NONE = 0
CU_MEM_HANDLE_TYPE_POSIX_FILE_DESCRIPTOR = 1
CU_MEM_HANDLE_TYPE_WIN32 = 2
CU_MEM_HANDLE_TYPE_WIN32_KMT = 4
CU_MEM_HANDLE_TYPE_FABRIC = 8
CU_MEM_HANDLE_TYPE_MAX = 2147483647
ctypedef CUmemAllocationHandleType_enum CUmemAllocationHandleType
cdef enum CUmemAccess_flags_enum:
CU_MEM_ACCESS_FLAGS_PROT_NONE = 0
CU_MEM_ACCESS_FLAGS_PROT_READ = 1
CU_MEM_ACCESS_FLAGS_PROT_READWRITE = 3
CU_MEM_ACCESS_FLAGS_PROT_MAX = 2147483647
ctypedef CUmemAccess_flags_enum CUmemAccess_flags
cdef enum CUmemLocationType_enum:
CU_MEM_LOCATION_TYPE_INVALID = 0
CU_MEM_LOCATION_TYPE_DEVICE = 1
CU_MEM_LOCATION_TYPE_HOST = 2
CU_MEM_LOCATION_TYPE_HOST_NUMA = 3
CU_MEM_LOCATION_TYPE_HOST_NUMA_CURRENT = 4
CU_MEM_LOCATION_TYPE_MAX = 2147483647
ctypedef CUmemLocationType_enum CUmemLocationType
cdef enum CUmemAllocationType_enum:
CU_MEM_ALLOCATION_TYPE_INVALID = 0
CU_MEM_ALLOCATION_TYPE_PINNED = 1
CU_MEM_ALLOCATION_TYPE_MAX = 2147483647
ctypedef CUmemAllocationType_enum CUmemAllocationType
cdef enum CUmemAllocationGranularity_flags_enum:
CU_MEM_ALLOC_GRANULARITY_MINIMUM = 0
CU_MEM_ALLOC_GRANULARITY_RECOMMENDED = 1
ctypedef CUmemAllocationGranularity_flags_enum CUmemAllocationGranularity_flags
cdef enum CUmemRangeHandleType_enum:
CU_MEM_RANGE_HANDLE_TYPE_DMA_BUF_FD = 1
CU_MEM_RANGE_HANDLE_TYPE_MAX = 2147483647
ctypedef CUmemRangeHandleType_enum CUmemRangeHandleType
cdef enum CUmemRangeFlags_enum:
CU_MEM_RANGE_FLAG_DMA_BUF_MAPPING_TYPE_PCIE = 1
ctypedef CUmemRangeFlags_enum CUmemRangeFlags
cdef enum CUarraySparseSubresourceType_enum:
CU_ARRAY_SPARSE_SUBRESOURCE_TYPE_SPARSE_LEVEL = 0
CU_ARRAY_SPARSE_SUBRESOURCE_TYPE_MIPTAIL = 1
ctypedef CUarraySparseSubresourceType_enum CUarraySparseSubresourceType
cdef enum CUmemOperationType_enum:
CU_MEM_OPERATION_TYPE_MAP = 1
CU_MEM_OPERATION_TYPE_UNMAP = 2
ctypedef CUmemOperationType_enum CUmemOperationType
cdef enum CUmemHandleType_enum:
CU_MEM_HANDLE_TYPE_GENERIC = 0
ctypedef CUmemHandleType_enum CUmemHandleType
cdef union anon_union9:
CUmipmappedArray mipmap
CUarray array
cdef struct anon_struct20:
unsigned int level
unsigned int layer
unsigned int offsetX
unsigned int offsetY
unsigned int offsetZ
unsigned int extentWidth
unsigned int extentHeight
unsigned int extentDepth
cdef struct anon_struct21:
unsigned int layer
unsigned long long offset
unsigned long long size
cdef union anon_union10:
anon_struct20 sparseLevel
anon_struct21 miptail
cdef union anon_union11:
CUmemGenericAllocationHandle memHandle
cdef struct CUarrayMapInfo_st:
CUresourcetype resourceType
anon_union9 resource
CUarraySparseSubresourceType subresourceType
anon_union10 subresource
CUmemOperationType memOperationType
CUmemHandleType memHandleType
anon_union11 memHandle
unsigned long long offset
unsigned int deviceBitMask
unsigned int flags
unsigned int reserved[2]
ctypedef CUarrayMapInfo_st CUarrayMapInfo_v1
ctypedef CUarrayMapInfo_v1 CUarrayMapInfo
cdef struct CUmemLocation_st:
CUmemLocationType type
int id
ctypedef CUmemLocation_st CUmemLocation_v1
ctypedef CUmemLocation_v1 CUmemLocation
cdef enum CUmemAllocationCompType_enum:
CU_MEM_ALLOCATION_COMP_NONE = 0
CU_MEM_ALLOCATION_COMP_GENERIC = 1
ctypedef CUmemAllocationCompType_enum CUmemAllocationCompType
cdef struct anon_struct22:
unsigned char compressionType
unsigned char gpuDirectRDMACapable
unsigned short usage
unsigned char reserved[4]
cdef struct CUmemAllocationProp_st:
CUmemAllocationType type
CUmemAllocationHandleType requestedHandleTypes
CUmemLocation location
void* win32HandleMetaData
anon_struct22 allocFlags
ctypedef CUmemAllocationProp_st CUmemAllocationProp_v1
ctypedef CUmemAllocationProp_v1 CUmemAllocationProp
cdef enum CUmulticastGranularity_flags_enum:
CU_MULTICAST_GRANULARITY_MINIMUM = 0
CU_MULTICAST_GRANULARITY_RECOMMENDED = 1
ctypedef CUmulticastGranularity_flags_enum CUmulticastGranularity_flags
cdef struct CUmulticastObjectProp_st:
unsigned int numDevices
size_t size
unsigned long long handleTypes
unsigned long long flags
ctypedef CUmulticastObjectProp_st CUmulticastObjectProp_v1
ctypedef CUmulticastObjectProp_v1 CUmulticastObjectProp
cdef struct CUmemAccessDesc_st:
CUmemLocation location
CUmemAccess_flags flags
ctypedef CUmemAccessDesc_st CUmemAccessDesc_v1
ctypedef CUmemAccessDesc_v1 CUmemAccessDesc
cdef enum CUgraphExecUpdateResult_enum:
CU_GRAPH_EXEC_UPDATE_SUCCESS = 0
CU_GRAPH_EXEC_UPDATE_ERROR = 1
CU_GRAPH_EXEC_UPDATE_ERROR_TOPOLOGY_CHANGED = 2
CU_GRAPH_EXEC_UPDATE_ERROR_NODE_TYPE_CHANGED = 3
CU_GRAPH_EXEC_UPDATE_ERROR_FUNCTION_CHANGED = 4
CU_GRAPH_EXEC_UPDATE_ERROR_PARAMETERS_CHANGED = 5
CU_GRAPH_EXEC_UPDATE_ERROR_NOT_SUPPORTED = 6
CU_GRAPH_EXEC_UPDATE_ERROR_UNSUPPORTED_FUNCTION_CHANGE = 7
CU_GRAPH_EXEC_UPDATE_ERROR_ATTRIBUTES_CHANGED = 8
ctypedef CUgraphExecUpdateResult_enum CUgraphExecUpdateResult
cdef struct CUgraphExecUpdateResultInfo_st:
CUgraphExecUpdateResult result
CUgraphNode errorNode
CUgraphNode errorFromNode
ctypedef CUgraphExecUpdateResultInfo_st CUgraphExecUpdateResultInfo_v1
ctypedef CUgraphExecUpdateResultInfo_v1 CUgraphExecUpdateResultInfo
cdef enum CUmemPool_attribute_enum:
CU_MEMPOOL_ATTR_REUSE_FOLLOW_EVENT_DEPENDENCIES = 1
CU_MEMPOOL_ATTR_REUSE_ALLOW_OPPORTUNISTIC = 2
CU_MEMPOOL_ATTR_REUSE_ALLOW_INTERNAL_DEPENDENCIES = 3
CU_MEMPOOL_ATTR_RELEASE_THRESHOLD = 4
CU_MEMPOOL_ATTR_RESERVED_MEM_CURRENT = 5
CU_MEMPOOL_ATTR_RESERVED_MEM_HIGH = 6
CU_MEMPOOL_ATTR_USED_MEM_CURRENT = 7
CU_MEMPOOL_ATTR_USED_MEM_HIGH = 8
ctypedef CUmemPool_attribute_enum CUmemPool_attribute
cdef struct CUmemPoolProps_st:
CUmemAllocationType allocType
CUmemAllocationHandleType handleTypes
CUmemLocation location
void* win32SecurityAttributes
size_t maxSize
unsigned short usage
unsigned char reserved[54]
ctypedef CUmemPoolProps_st CUmemPoolProps_v1
ctypedef CUmemPoolProps_v1 CUmemPoolProps
cdef struct CUmemPoolPtrExportData_st:
unsigned char reserved[64]
ctypedef CUmemPoolPtrExportData_st CUmemPoolPtrExportData_v1
ctypedef CUmemPoolPtrExportData_v1 CUmemPoolPtrExportData
cdef enum CUmemcpyFlags_enum:
CU_MEMCPY_FLAG_DEFAULT = 0
CU_MEMCPY_FLAG_PREFER_OVERLAP_WITH_COMPUTE = 1
ctypedef CUmemcpyFlags_enum CUmemcpyFlags
cdef enum CUmemcpySrcAccessOrder_enum:
CU_MEMCPY_SRC_ACCESS_ORDER_INVALID = 0
CU_MEMCPY_SRC_ACCESS_ORDER_STREAM = 1
CU_MEMCPY_SRC_ACCESS_ORDER_DURING_API_CALL = 2
CU_MEMCPY_SRC_ACCESS_ORDER_ANY = 3
CU_MEMCPY_SRC_ACCESS_ORDER_MAX = 2147483647
ctypedef CUmemcpySrcAccessOrder_enum CUmemcpySrcAccessOrder
cdef struct CUmemcpyAttributes_st:
CUmemcpySrcAccessOrder srcAccessOrder
CUmemLocation srcLocHint
CUmemLocation dstLocHint
unsigned int flags
ctypedef CUmemcpyAttributes_st CUmemcpyAttributes_v1
ctypedef CUmemcpyAttributes_v1 CUmemcpyAttributes
cdef enum CUmemcpy3DOperandType_enum:
CU_MEMCPY_OPERAND_TYPE_POINTER = 1
CU_MEMCPY_OPERAND_TYPE_ARRAY = 2
CU_MEMCPY_OPERAND_TYPE_MAX = 2147483647
ctypedef CUmemcpy3DOperandType_enum CUmemcpy3DOperandType
cdef struct CUoffset3D_st:
size_t x
size_t y
size_t z
ctypedef CUoffset3D_st CUoffset3D_v1
ctypedef CUoffset3D_v1 CUoffset3D
cdef struct CUextent3D_st:
size_t width
size_t height
size_t depth
ctypedef CUextent3D_st CUextent3D_v1
ctypedef CUextent3D_v1 CUextent3D
cdef struct anon_struct23:
CUdeviceptr ptr
size_t rowLength
size_t layerHeight
CUmemLocation locHint
cdef struct anon_struct24:
CUarray array
CUoffset3D offset
cdef union anon_union12:
anon_struct23 ptr
anon_struct24 array
cdef struct CUmemcpy3DOperand_st:
CUmemcpy3DOperandType type
anon_union12 op
ctypedef CUmemcpy3DOperand_st CUmemcpy3DOperand_v1
ctypedef CUmemcpy3DOperand_v1 CUmemcpy3DOperand
cdef struct CUDA_MEMCPY3D_BATCH_OP_st:
CUmemcpy3DOperand src
CUmemcpy3DOperand dst
CUextent3D extent
CUmemcpySrcAccessOrder srcAccessOrder
unsigned int flags
ctypedef CUDA_MEMCPY3D_BATCH_OP_st CUDA_MEMCPY3D_BATCH_OP_v1
ctypedef CUDA_MEMCPY3D_BATCH_OP_v1 CUDA_MEMCPY3D_BATCH_OP
cdef struct CUDA_MEM_ALLOC_NODE_PARAMS_v1_st:
CUmemPoolProps poolProps
const CUmemAccessDesc* accessDescs
size_t accessDescCount
size_t bytesize
CUdeviceptr dptr
ctypedef CUDA_MEM_ALLOC_NODE_PARAMS_v1_st CUDA_MEM_ALLOC_NODE_PARAMS_v1
ctypedef CUDA_MEM_ALLOC_NODE_PARAMS_v1 CUDA_MEM_ALLOC_NODE_PARAMS
cdef struct CUDA_MEM_ALLOC_NODE_PARAMS_v2_st:
CUmemPoolProps poolProps
const CUmemAccessDesc* accessDescs
size_t accessDescCount
size_t bytesize
CUdeviceptr dptr
ctypedef CUDA_MEM_ALLOC_NODE_PARAMS_v2_st CUDA_MEM_ALLOC_NODE_PARAMS_v2
cdef struct CUDA_MEM_FREE_NODE_PARAMS_st:
CUdeviceptr dptr
ctypedef CUDA_MEM_FREE_NODE_PARAMS_st CUDA_MEM_FREE_NODE_PARAMS
cdef enum CUgraphMem_attribute_enum:
CU_GRAPH_MEM_ATTR_USED_MEM_CURRENT = 0
CU_GRAPH_MEM_ATTR_USED_MEM_HIGH = 1
CU_GRAPH_MEM_ATTR_RESERVED_MEM_CURRENT = 2
CU_GRAPH_MEM_ATTR_RESERVED_MEM_HIGH = 3
ctypedef CUgraphMem_attribute_enum CUgraphMem_attribute
cdef enum CUgraphChildGraphNodeOwnership_enum:
CU_GRAPH_CHILD_GRAPH_OWNERSHIP_CLONE = 0
CU_GRAPH_CHILD_GRAPH_OWNERSHIP_MOVE = 1
ctypedef CUgraphChildGraphNodeOwnership_enum CUgraphChildGraphNodeOwnership
cdef struct CUDA_CHILD_GRAPH_NODE_PARAMS_st:
CUgraph graph
CUgraphChildGraphNodeOwnership ownership
ctypedef CUDA_CHILD_GRAPH_NODE_PARAMS_st CUDA_CHILD_GRAPH_NODE_PARAMS
cdef struct CUDA_EVENT_RECORD_NODE_PARAMS_st:
CUevent event
ctypedef CUDA_EVENT_RECORD_NODE_PARAMS_st CUDA_EVENT_RECORD_NODE_PARAMS
cdef struct CUDA_EVENT_WAIT_NODE_PARAMS_st:
CUevent event
ctypedef CUDA_EVENT_WAIT_NODE_PARAMS_st CUDA_EVENT_WAIT_NODE_PARAMS
cdef struct CUgraphNodeParams_st:
CUgraphNodeType type
int reserved0[3]
long long reserved1[29]
CUDA_KERNEL_NODE_PARAMS_v3 kernel
CUDA_MEMCPY_NODE_PARAMS memcpy
CUDA_MEMSET_NODE_PARAMS_v2 memset
CUDA_HOST_NODE_PARAMS_v2 host
CUDA_CHILD_GRAPH_NODE_PARAMS graph
CUDA_EVENT_WAIT_NODE_PARAMS eventWait
CUDA_EVENT_RECORD_NODE_PARAMS eventRecord
CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2 extSemSignal
CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2 extSemWait
CUDA_MEM_ALLOC_NODE_PARAMS_v2 alloc
CUDA_MEM_FREE_NODE_PARAMS free
CUDA_BATCH_MEM_OP_NODE_PARAMS_v2 memOp
CUDA_CONDITIONAL_NODE_PARAMS conditional
long long reserved2
ctypedef CUgraphNodeParams_st CUgraphNodeParams
cdef enum CUflushGPUDirectRDMAWritesOptions_enum:
CU_FLUSH_GPU_DIRECT_RDMA_WRITES_OPTION_HOST = 1
CU_FLUSH_GPU_DIRECT_RDMA_WRITES_OPTION_MEMOPS = 2
ctypedef CUflushGPUDirectRDMAWritesOptions_enum CUflushGPUDirectRDMAWritesOptions
cdef enum CUGPUDirectRDMAWritesOrdering_enum:
CU_GPU_DIRECT_RDMA_WRITES_ORDERING_NONE = 0
CU_GPU_DIRECT_RDMA_WRITES_ORDERING_OWNER = 100
CU_GPU_DIRECT_RDMA_WRITES_ORDERING_ALL_DEVICES = 200
ctypedef CUGPUDirectRDMAWritesOrdering_enum CUGPUDirectRDMAWritesOrdering
cdef enum CUflushGPUDirectRDMAWritesScope_enum:
CU_FLUSH_GPU_DIRECT_RDMA_WRITES_TO_OWNER = 100
CU_FLUSH_GPU_DIRECT_RDMA_WRITES_TO_ALL_DEVICES = 200
ctypedef CUflushGPUDirectRDMAWritesScope_enum CUflushGPUDirectRDMAWritesScope
cdef enum CUflushGPUDirectRDMAWritesTarget_enum:
CU_FLUSH_GPU_DIRECT_RDMA_WRITES_TARGET_CURRENT_CTX = 0
ctypedef CUflushGPUDirectRDMAWritesTarget_enum CUflushGPUDirectRDMAWritesTarget
cdef enum CUgraphDebugDot_flags_enum:
CU_GRAPH_DEBUG_DOT_FLAGS_VERBOSE = 1
CU_GRAPH_DEBUG_DOT_FLAGS_RUNTIME_TYPES = 2
CU_GRAPH_DEBUG_DOT_FLAGS_KERNEL_NODE_PARAMS = 4
CU_GRAPH_DEBUG_DOT_FLAGS_MEMCPY_NODE_PARAMS = 8
CU_GRAPH_DEBUG_DOT_FLAGS_MEMSET_NODE_PARAMS = 16
CU_GRAPH_DEBUG_DOT_FLAGS_HOST_NODE_PARAMS = 32
CU_GRAPH_DEBUG_DOT_FLAGS_EVENT_NODE_PARAMS = 64
CU_GRAPH_DEBUG_DOT_FLAGS_EXT_SEMAS_SIGNAL_NODE_PARAMS = 128
CU_GRAPH_DEBUG_DOT_FLAGS_EXT_SEMAS_WAIT_NODE_PARAMS = 256
CU_GRAPH_DEBUG_DOT_FLAGS_KERNEL_NODE_ATTRIBUTES = 512
CU_GRAPH_DEBUG_DOT_FLAGS_HANDLES = 1024
CU_GRAPH_DEBUG_DOT_FLAGS_MEM_ALLOC_NODE_PARAMS = 2048
CU_GRAPH_DEBUG_DOT_FLAGS_MEM_FREE_NODE_PARAMS = 4096
CU_GRAPH_DEBUG_DOT_FLAGS_BATCH_MEM_OP_NODE_PARAMS = 8192
CU_GRAPH_DEBUG_DOT_FLAGS_EXTRA_TOPO_INFO = 16384
CU_GRAPH_DEBUG_DOT_FLAGS_CONDITIONAL_NODE_PARAMS = 32768
ctypedef CUgraphDebugDot_flags_enum CUgraphDebugDot_flags
cdef enum CUuserObject_flags_enum:
CU_USER_OBJECT_NO_DESTRUCTOR_SYNC = 1
ctypedef CUuserObject_flags_enum CUuserObject_flags
cdef enum CUuserObjectRetain_flags_enum:
CU_GRAPH_USER_OBJECT_MOVE = 1
ctypedef CUuserObjectRetain_flags_enum CUuserObjectRetain_flags
cdef enum CUgraphInstantiate_flags_enum:
CUDA_GRAPH_INSTANTIATE_FLAG_AUTO_FREE_ON_LAUNCH = 1
CUDA_GRAPH_INSTANTIATE_FLAG_UPLOAD = 2
CUDA_GRAPH_INSTANTIATE_FLAG_DEVICE_LAUNCH = 4
CUDA_GRAPH_INSTANTIATE_FLAG_USE_NODE_PRIORITY = 8
ctypedef CUgraphInstantiate_flags_enum CUgraphInstantiate_flags
cdef enum CUdeviceNumaConfig_enum:
CU_DEVICE_NUMA_CONFIG_NONE = 0
CU_DEVICE_NUMA_CONFIG_NUMA_NODE = 1
ctypedef CUdeviceNumaConfig_enum CUdeviceNumaConfig
cdef enum CUprocessState_enum:
CU_PROCESS_STATE_RUNNING = 0
CU_PROCESS_STATE_LOCKED = 1
CU_PROCESS_STATE_CHECKPOINTED = 2
CU_PROCESS_STATE_FAILED = 3
ctypedef CUprocessState_enum CUprocessState
cdef struct CUcheckpointLockArgs_st:
unsigned int timeoutMs
unsigned int reserved0
cuuint64_t reserved1[7]
ctypedef CUcheckpointLockArgs_st CUcheckpointLockArgs
cdef struct CUcheckpointCheckpointArgs_st:
cuuint64_t reserved[8]
ctypedef CUcheckpointCheckpointArgs_st CUcheckpointCheckpointArgs
cdef struct CUcheckpointRestoreArgs_st:
cuuint64_t reserved[8]
ctypedef CUcheckpointRestoreArgs_st CUcheckpointRestoreArgs
cdef struct CUcheckpointUnlockArgs_st:
cuuint64_t reserved[8]
ctypedef CUcheckpointUnlockArgs_st CUcheckpointUnlockArgs
cdef enum CUmoduleLoadingMode_enum:
CU_MODULE_EAGER_LOADING = 1
CU_MODULE_LAZY_LOADING = 2
ctypedef CUmoduleLoadingMode_enum CUmoduleLoadingMode
cdef enum CUmemDecompressAlgorithm_enum:
CU_MEM_DECOMPRESS_UNSUPPORTED = 0
CU_MEM_DECOMPRESS_ALGORITHM_DEFLATE = 1
CU_MEM_DECOMPRESS_ALGORITHM_SNAPPY = 2
CU_MEM_DECOMPRESS_ALGORITHM_LZ4 = 4
ctypedef CUmemDecompressAlgorithm_enum CUmemDecompressAlgorithm
cdef struct CUmemDecompressParams_st:
size_t srcNumBytes
size_t dstNumBytes
cuuint32_t* dstActBytes
const void* src
void* dst
CUmemDecompressAlgorithm algo
unsigned char padding[20]
ctypedef CUmemDecompressParams_st CUmemDecompressParams
cdef enum CUfunctionLoadingState_enum:
CU_FUNCTION_LOADING_STATE_UNLOADED = 0
CU_FUNCTION_LOADING_STATE_LOADED = 1
CU_FUNCTION_LOADING_STATE_MAX = 2
ctypedef CUfunctionLoadingState_enum CUfunctionLoadingState
cdef enum CUcoredumpSettings_enum:
CU_COREDUMP_ENABLE_ON_EXCEPTION = 1
CU_COREDUMP_TRIGGER_HOST = 2
CU_COREDUMP_LIGHTWEIGHT = 3
CU_COREDUMP_ENABLE_USER_TRIGGER = 4
CU_COREDUMP_FILE = 5
CU_COREDUMP_PIPE = 6
CU_COREDUMP_GENERATION_FLAGS = 7
CU_COREDUMP_MAX = 8
ctypedef CUcoredumpSettings_enum CUcoredumpSettings
cdef enum CUCoredumpGenerationFlags:
CU_COREDUMP_DEFAULT_FLAGS = 0
CU_COREDUMP_SKIP_NONRELOCATED_ELF_IMAGES = 1
CU_COREDUMP_SKIP_GLOBAL_MEMORY = 2
CU_COREDUMP_SKIP_SHARED_MEMORY = 4
CU_COREDUMP_SKIP_LOCAL_MEMORY = 8
CU_COREDUMP_SKIP_ABORT = 16
CU_COREDUMP_SKIP_CONSTBANK_MEMORY = 32
CU_COREDUMP_LIGHTWEIGHT_FLAGS = 47
cdef struct CUdevResourceDesc_st:
pass
ctypedef CUdevResourceDesc_st* CUdevResourceDesc
ctypedef enum CUgreenCtxCreate_flags:
CU_GREEN_CTX_DEFAULT_STREAM = 1
ctypedef enum CUdevSmResourceSplit_flags:
CU_DEV_SM_RESOURCE_SPLIT_IGNORE_SM_COSCHEDULING = 1
CU_DEV_SM_RESOURCE_SPLIT_MAX_POTENTIAL_CLUSTER_SIZE = 2
ctypedef enum CUdevResourceType:
CU_DEV_RESOURCE_TYPE_INVALID = 0
CU_DEV_RESOURCE_TYPE_SM = 1
cdef struct CUdevSmResource_st:
unsigned int smCount
ctypedef CUdevSmResource_st CUdevSmResource
cdef struct CUdevResource_st:
CUdevResourceType type
unsigned char _internal_padding[92]
CUdevSmResource sm
unsigned char _oversize[48]
ctypedef CUdevResource_st CUdevResource_v1
ctypedef CUdevResource_v1 CUdevResource
cdef enum CUlogLevel_enum:
CU_LOG_LEVEL_ERROR = 0
CU_LOG_LEVEL_WARNING = 1
ctypedef CUlogLevel_enum CUlogLevel
cdef struct CUlogsCallbackEntry_st:
pass
ctypedef CUlogsCallbackEntry_st* CUlogsCallbackHandle
ctypedef void (*CUlogsCallback)(void* data, CUlogLevel logLevel, char* message, size_t length)
ctypedef unsigned int CUlogIterator
cdef extern from "cudaProfiler.h":
cdef enum CUoutput_mode_enum:
CU_OUT_KEY_VALUE_PAIR = 0
CU_OUT_CSV = 1
ctypedef CUoutput_mode_enum CUoutput_mode
cdef enum CUeglFrameType_enum:
CU_EGL_FRAME_TYPE_ARRAY = 0
CU_EGL_FRAME_TYPE_PITCH = 1
ctypedef CUeglFrameType_enum CUeglFrameType
cdef enum CUeglResourceLocationFlags_enum:
CU_EGL_RESOURCE_LOCATION_SYSMEM = 0
CU_EGL_RESOURCE_LOCATION_VIDMEM = 1
ctypedef CUeglResourceLocationFlags_enum CUeglResourceLocationFlags
cdef enum CUeglColorFormat_enum:
CU_EGL_COLOR_FORMAT_YUV420_PLANAR = 0
CU_EGL_COLOR_FORMAT_YUV420_SEMIPLANAR = 1
CU_EGL_COLOR_FORMAT_YUV422_PLANAR = 2
CU_EGL_COLOR_FORMAT_YUV422_SEMIPLANAR = 3
CU_EGL_COLOR_FORMAT_RGB = 4
CU_EGL_COLOR_FORMAT_BGR = 5
CU_EGL_COLOR_FORMAT_ARGB = 6
CU_EGL_COLOR_FORMAT_RGBA = 7
CU_EGL_COLOR_FORMAT_L = 8
CU_EGL_COLOR_FORMAT_R = 9
CU_EGL_COLOR_FORMAT_YUV444_PLANAR = 10
CU_EGL_COLOR_FORMAT_YUV444_SEMIPLANAR = 11
CU_EGL_COLOR_FORMAT_YUYV_422 = 12
CU_EGL_COLOR_FORMAT_UYVY_422 = 13
CU_EGL_COLOR_FORMAT_ABGR = 14
CU_EGL_COLOR_FORMAT_BGRA = 15
CU_EGL_COLOR_FORMAT_A = 16
CU_EGL_COLOR_FORMAT_RG = 17
CU_EGL_COLOR_FORMAT_AYUV = 18
CU_EGL_COLOR_FORMAT_YVU444_SEMIPLANAR = 19
CU_EGL_COLOR_FORMAT_YVU422_SEMIPLANAR = 20
CU_EGL_COLOR_FORMAT_YVU420_SEMIPLANAR = 21
CU_EGL_COLOR_FORMAT_Y10V10U10_444_SEMIPLANAR = 22
CU_EGL_COLOR_FORMAT_Y10V10U10_420_SEMIPLANAR = 23
CU_EGL_COLOR_FORMAT_Y12V12U12_444_SEMIPLANAR = 24
CU_EGL_COLOR_FORMAT_Y12V12U12_420_SEMIPLANAR = 25
CU_EGL_COLOR_FORMAT_VYUY_ER = 26
CU_EGL_COLOR_FORMAT_UYVY_ER = 27
CU_EGL_COLOR_FORMAT_YUYV_ER = 28
CU_EGL_COLOR_FORMAT_YVYU_ER = 29
CU_EGL_COLOR_FORMAT_YUV_ER = 30
CU_EGL_COLOR_FORMAT_YUVA_ER = 31
CU_EGL_COLOR_FORMAT_AYUV_ER = 32
CU_EGL_COLOR_FORMAT_YUV444_PLANAR_ER = 33
CU_EGL_COLOR_FORMAT_YUV422_PLANAR_ER = 34
CU_EGL_COLOR_FORMAT_YUV420_PLANAR_ER = 35
CU_EGL_COLOR_FORMAT_YUV444_SEMIPLANAR_ER = 36
CU_EGL_COLOR_FORMAT_YUV422_SEMIPLANAR_ER = 37
CU_EGL_COLOR_FORMAT_YUV420_SEMIPLANAR_ER = 38
CU_EGL_COLOR_FORMAT_YVU444_PLANAR_ER = 39
CU_EGL_COLOR_FORMAT_YVU422_PLANAR_ER = 40
CU_EGL_COLOR_FORMAT_YVU420_PLANAR_ER = 41
CU_EGL_COLOR_FORMAT_YVU444_SEMIPLANAR_ER = 42
CU_EGL_COLOR_FORMAT_YVU422_SEMIPLANAR_ER = 43
CU_EGL_COLOR_FORMAT_YVU420_SEMIPLANAR_ER = 44
CU_EGL_COLOR_FORMAT_BAYER_RGGB = 45
CU_EGL_COLOR_FORMAT_BAYER_BGGR = 46
CU_EGL_COLOR_FORMAT_BAYER_GRBG = 47
CU_EGL_COLOR_FORMAT_BAYER_GBRG = 48
CU_EGL_COLOR_FORMAT_BAYER10_RGGB = 49
CU_EGL_COLOR_FORMAT_BAYER10_BGGR = 50
CU_EGL_COLOR_FORMAT_BAYER10_GRBG = 51
CU_EGL_COLOR_FORMAT_BAYER10_GBRG = 52
CU_EGL_COLOR_FORMAT_BAYER12_RGGB = 53
CU_EGL_COLOR_FORMAT_BAYER12_BGGR = 54
CU_EGL_COLOR_FORMAT_BAYER12_GRBG = 55
CU_EGL_COLOR_FORMAT_BAYER12_GBRG = 56
CU_EGL_COLOR_FORMAT_BAYER14_RGGB = 57
CU_EGL_COLOR_FORMAT_BAYER14_BGGR = 58
CU_EGL_COLOR_FORMAT_BAYER14_GRBG = 59
CU_EGL_COLOR_FORMAT_BAYER14_GBRG = 60
CU_EGL_COLOR_FORMAT_BAYER20_RGGB = 61
CU_EGL_COLOR_FORMAT_BAYER20_BGGR = 62
CU_EGL_COLOR_FORMAT_BAYER20_GRBG = 63
CU_EGL_COLOR_FORMAT_BAYER20_GBRG = 64
CU_EGL_COLOR_FORMAT_YVU444_PLANAR = 65
CU_EGL_COLOR_FORMAT_YVU422_PLANAR = 66
CU_EGL_COLOR_FORMAT_YVU420_PLANAR = 67
CU_EGL_COLOR_FORMAT_BAYER_ISP_RGGB = 68
CU_EGL_COLOR_FORMAT_BAYER_ISP_BGGR = 69
CU_EGL_COLOR_FORMAT_BAYER_ISP_GRBG = 70
CU_EGL_COLOR_FORMAT_BAYER_ISP_GBRG = 71
CU_EGL_COLOR_FORMAT_BAYER_BCCR = 72
CU_EGL_COLOR_FORMAT_BAYER_RCCB = 73
CU_EGL_COLOR_FORMAT_BAYER_CRBC = 74
CU_EGL_COLOR_FORMAT_BAYER_CBRC = 75
CU_EGL_COLOR_FORMAT_BAYER10_CCCC = 76
CU_EGL_COLOR_FORMAT_BAYER12_BCCR = 77
CU_EGL_COLOR_FORMAT_BAYER12_RCCB = 78
CU_EGL_COLOR_FORMAT_BAYER12_CRBC = 79
CU_EGL_COLOR_FORMAT_BAYER12_CBRC = 80
CU_EGL_COLOR_FORMAT_BAYER12_CCCC = 81
CU_EGL_COLOR_FORMAT_Y = 82
CU_EGL_COLOR_FORMAT_YUV420_SEMIPLANAR_2020 = 83
CU_EGL_COLOR_FORMAT_YVU420_SEMIPLANAR_2020 = 84
CU_EGL_COLOR_FORMAT_YUV420_PLANAR_2020 = 85
CU_EGL_COLOR_FORMAT_YVU420_PLANAR_2020 = 86
CU_EGL_COLOR_FORMAT_YUV420_SEMIPLANAR_709 = 87
CU_EGL_COLOR_FORMAT_YVU420_SEMIPLANAR_709 = 88
CU_EGL_COLOR_FORMAT_YUV420_PLANAR_709 = 89
CU_EGL_COLOR_FORMAT_YVU420_PLANAR_709 = 90
CU_EGL_COLOR_FORMAT_Y10V10U10_420_SEMIPLANAR_709 = 91
CU_EGL_COLOR_FORMAT_Y10V10U10_420_SEMIPLANAR_2020 = 92
CU_EGL_COLOR_FORMAT_Y10V10U10_422_SEMIPLANAR_2020 = 93
CU_EGL_COLOR_FORMAT_Y10V10U10_422_SEMIPLANAR = 94
CU_EGL_COLOR_FORMAT_Y10V10U10_422_SEMIPLANAR_709 = 95
CU_EGL_COLOR_FORMAT_Y_ER = 96
CU_EGL_COLOR_FORMAT_Y_709_ER = 97
CU_EGL_COLOR_FORMAT_Y10_ER = 98
CU_EGL_COLOR_FORMAT_Y10_709_ER = 99
CU_EGL_COLOR_FORMAT_Y12_ER = 100
CU_EGL_COLOR_FORMAT_Y12_709_ER = 101
CU_EGL_COLOR_FORMAT_YUVA = 102
CU_EGL_COLOR_FORMAT_YUV = 103
CU_EGL_COLOR_FORMAT_YVYU = 104
CU_EGL_COLOR_FORMAT_VYUY = 105
CU_EGL_COLOR_FORMAT_Y10V10U10_420_SEMIPLANAR_ER = 106
CU_EGL_COLOR_FORMAT_Y10V10U10_420_SEMIPLANAR_709_ER = 107
CU_EGL_COLOR_FORMAT_Y10V10U10_444_SEMIPLANAR_ER = 108
CU_EGL_COLOR_FORMAT_Y10V10U10_444_SEMIPLANAR_709_ER = 109
CU_EGL_COLOR_FORMAT_Y12V12U12_420_SEMIPLANAR_ER = 110
CU_EGL_COLOR_FORMAT_Y12V12U12_420_SEMIPLANAR_709_ER = 111
CU_EGL_COLOR_FORMAT_Y12V12U12_444_SEMIPLANAR_ER = 112
CU_EGL_COLOR_FORMAT_Y12V12U12_444_SEMIPLANAR_709_ER = 113
CU_EGL_COLOR_FORMAT_UYVY_709 = 114
CU_EGL_COLOR_FORMAT_UYVY_709_ER = 115
CU_EGL_COLOR_FORMAT_UYVY_2020 = 116
CU_EGL_COLOR_FORMAT_MAX = 117
ctypedef CUeglColorFormat_enum CUeglColorFormat
cdef union anon_union15:
CUarray pArray[3]
void* pPitch[3]
cdef struct CUeglFrame_st:
anon_union15 frame
unsigned int width
unsigned int height
unsigned int depth
unsigned int pitch
unsigned int planeCount
unsigned int numChannels
CUeglFrameType frameType
CUeglColorFormat eglColorFormat
CUarray_format cuFormat
ctypedef CUeglFrame_st CUeglFrame_v1
ctypedef CUeglFrame_v1 CUeglFrame
cdef extern from "":
cdef struct CUeglStreamConnection_st:
pass
ctypedef CUeglStreamConnection_st* CUeglStreamConnection
cdef enum CUGLDeviceList_enum:
CU_GL_DEVICE_LIST_ALL = 1
CU_GL_DEVICE_LIST_CURRENT_FRAME = 2
CU_GL_DEVICE_LIST_NEXT_FRAME = 3
ctypedef CUGLDeviceList_enum CUGLDeviceList
cdef enum CUGLmap_flags_enum:
CU_GL_MAP_RESOURCE_FLAGS_NONE = 0
CU_GL_MAP_RESOURCE_FLAGS_READ_ONLY = 1
CU_GL_MAP_RESOURCE_FLAGS_WRITE_DISCARD = 2
ctypedef CUGLmap_flags_enum CUGLmap_flags
ctypedef unsigned int GLenum
ctypedef unsigned int GLuint
cdef extern from "":
cdef struct void:
pass
ctypedef void* EGLImageKHR
cdef extern from "":
cdef struct void:
pass
ctypedef void* EGLStreamKHR
ctypedef unsigned int EGLint
cdef extern from "":
cdef struct void:
pass
ctypedef void* EGLSyncKHR
ctypedef uint32_t VdpDevice
ctypedef unsigned long long VdpGetProcAddress
ctypedef uint32_t VdpVideoSurface
ctypedef uint32_t VdpOutputSurface
cdef CUresult cuGetErrorString(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGetErrorName(CUresult error, const char** pStr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuInit(unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDriverGetVersion(int* driverVersion) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGet(CUdevice* device, int ordinal) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetCount(int* count) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetName(char* name, int length, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetUuid(CUuuid* uuid, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetUuid_v2(CUuuid* uuid, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetLuid(char* luid, unsigned int* deviceNodeMask, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceTotalMem(size_t* numbytes, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetTexture1DLinearMaxWidth(size_t* maxWidthInElements, CUarray_format pformat, unsigned numChannels, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetAttribute(int* pi, CUdevice_attribute attrib, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetNvSciSyncAttributes(void* nvSciSyncAttrList, CUdevice dev, int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceSetMemPool(CUdevice dev, CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetMemPool(CUmemoryPool* pool, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetDefaultMemPool(CUmemoryPool* pool_out, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetExecAffinitySupport(int* pi, CUexecAffinityType typename, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFlushGPUDirectRDMAWrites(CUflushGPUDirectRDMAWritesTarget target, CUflushGPUDirectRDMAWritesScope scope) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetProperties(CUdevprop* prop, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceComputeCapability(int* major, int* minor, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDevicePrimaryCtxRetain(CUcontext* pctx, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDevicePrimaryCtxRelease(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDevicePrimaryCtxSetFlags(CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDevicePrimaryCtxGetState(CUdevice dev, unsigned int* flags, int* active) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDevicePrimaryCtxReset(CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxCreate(CUcontext* pctx, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxCreate_v3(CUcontext* pctx, CUexecAffinityParam* paramsArray, int numParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxCreate_v4(CUcontext* pctx, CUctxCreateParams* ctxCreateParams, unsigned int flags, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxDestroy(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxPushCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxPopCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxSetCurrent(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetCurrent(CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetDevice(CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetFlags(unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxSetFlags(unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetId(CUcontext ctx, unsigned long long* ctxId) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxSynchronize() except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxSetLimit(CUlimit limit, size_t value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetLimit(size_t* pvalue, CUlimit limit) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetCacheConfig(CUfunc_cache* pconfig) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxSetCacheConfig(CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetApiVersion(CUcontext ctx, unsigned int* version) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetStreamPriorityRange(int* leastPriority, int* greatestPriority) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxResetPersistingL2Cache() except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetExecAffinity(CUexecAffinityParam* pExecAffinity, CUexecAffinityType typename) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxRecordEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxWaitEvent(CUcontext hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxAttach(CUcontext* pctx, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxDetach(CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetSharedMemConfig(CUsharedconfig* pConfig) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxSetSharedMemConfig(CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleLoad(CUmodule* module, const char* fname) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleLoadData(CUmodule* module, const void* image) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleLoadDataEx(CUmodule* module, const void* image, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleLoadFatBinary(CUmodule* module, const void* fatCubin) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleUnload(CUmodule hmod) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleGetLoadingMode(CUmoduleLoadingMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleGetFunction(CUfunction* hfunc, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleGetFunctionCount(unsigned int* count, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleEnumerateFunctions(CUfunction* functions, unsigned int numFunctions, CUmodule mod) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleGetGlobal(CUdeviceptr* dptr, size_t* numbytes, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLinkCreate(unsigned int numOptions, CUjit_option* options, void** optionValues, CUlinkState* stateOut) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLinkAddData(CUlinkState state, CUjitInputType typename, void* data, size_t size, const char* name, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLinkAddFile(CUlinkState state, CUjitInputType typename, const char* path, unsigned int numOptions, CUjit_option* options, void** optionValues) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLinkComplete(CUlinkState state, void** cubinOut, size_t* sizeOut) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLinkDestroy(CUlinkState state) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleGetTexRef(CUtexref* pTexRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuModuleGetSurfRef(CUsurfref* pSurfRef, CUmodule hmod, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef 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
cdef CUresult cuLibraryUnload(CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLibraryGetKernel(CUkernel* pKernel, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLibraryGetKernelCount(unsigned int* count, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLibraryEnumerateKernels(CUkernel* kernels, unsigned int numKernels, CUlibrary lib) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLibraryGetModule(CUmodule* pMod, CUlibrary library) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuKernelGetFunction(CUfunction* pFunc, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuKernelGetLibrary(CUlibrary* pLib, CUkernel kernel) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLibraryGetGlobal(CUdeviceptr* dptr, size_t* numbytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLibraryGetManaged(CUdeviceptr* dptr, size_t* numbytes, CUlibrary library, const char* name) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLibraryGetUnifiedFunction(void** fptr, CUlibrary library, const char* symbol) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuKernelGetAttribute(int* pi, CUfunction_attribute attrib, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuKernelSetAttribute(CUfunction_attribute attrib, int val, CUkernel kernel, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuKernelSetCacheConfig(CUkernel kernel, CUfunc_cache config, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuKernelGetName(const char** name, CUkernel hfunc) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuKernelGetParamInfo(CUkernel kernel, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemGetInfo(size_t* free, size_t* total) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAlloc(CUdeviceptr* dptr, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAllocPitch(CUdeviceptr* dptr, size_t* pPitch, size_t WidthInBytes, size_t Height, unsigned int ElementSizeBytes) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemFree(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemGetAddressRange(CUdeviceptr* pbase, size_t* psize, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAllocHost(void** pp, size_t bytesize) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemFreeHost(void* p) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemHostAlloc(void** pp, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemHostGetDevicePointer(CUdeviceptr* pdptr, void* p, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemHostGetFlags(unsigned int* pFlags, void* p) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAllocManaged(CUdeviceptr* dptr, size_t bytesize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceRegisterAsyncNotification(CUdevice device, CUasyncCallback callbackFunc, void* userData, CUasyncCallbackHandle* callback) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceUnregisterAsyncNotification(CUdevice device, CUasyncCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetByPCIBusId(CUdevice* dev, const char* pciBusId) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetPCIBusId(char* pciBusId, int length, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuIpcGetEventHandle(CUipcEventHandle* pHandle, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuIpcOpenEventHandle(CUevent* phEvent, CUipcEventHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuIpcGetMemHandle(CUipcMemHandle* pHandle, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuIpcOpenMemHandle(CUdeviceptr* pdptr, CUipcMemHandle handle, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuIpcCloseMemHandle(CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemHostRegister(void* p, size_t bytesize, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemHostUnregister(void* p) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpy(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyPeer(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyHtoD(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyDtoH(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyDtoD(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyDtoA(CUarray dstArray, size_t dstOffset, CUdeviceptr srcDevice, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyAtoD(CUdeviceptr dstDevice, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyHtoA(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyAtoH(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyAtoA(CUarray dstArray, size_t dstOffset, CUarray srcArray, size_t srcOffset, size_t ByteCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpy2D(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpy2DUnaligned(const CUDA_MEMCPY2D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpy3D(const CUDA_MEMCPY3D* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpy3DPeer(const CUDA_MEMCPY3D_PEER* pCopy) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyAsync(CUdeviceptr dst, CUdeviceptr src, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyPeerAsync(CUdeviceptr dstDevice, CUcontext dstContext, CUdeviceptr srcDevice, CUcontext srcContext, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyHtoDAsync(CUdeviceptr dstDevice, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyDtoHAsync(void* dstHost, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyDtoDAsync(CUdeviceptr dstDevice, CUdeviceptr srcDevice, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyHtoAAsync(CUarray dstArray, size_t dstOffset, const void* srcHost, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyAtoHAsync(void* dstHost, CUarray srcArray, size_t srcOffset, size_t ByteCount, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpy2DAsync(const CUDA_MEMCPY2D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpy3DAsync(const CUDA_MEMCPY3D* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpy3DPeerAsync(const CUDA_MEMCPY3D_PEER* pCopy, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpyBatchAsync(CUdeviceptr* dsts, CUdeviceptr* srcs, size_t* sizes, size_t count, CUmemcpyAttributes* attrs, size_t* attrsIdxs, size_t numAttrs, size_t* failIdx, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemcpy3DBatchAsync(size_t numOps, CUDA_MEMCPY3D_BATCH_OP* opList, size_t* failIdx, unsigned long long flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD8(CUdeviceptr dstDevice, unsigned char uc, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD16(CUdeviceptr dstDevice, unsigned short us, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD32(CUdeviceptr dstDevice, unsigned int ui, size_t N) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD2D8(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD2D16(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD2D32(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD8Async(CUdeviceptr dstDevice, unsigned char uc, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD16Async(CUdeviceptr dstDevice, unsigned short us, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD32Async(CUdeviceptr dstDevice, unsigned int ui, size_t N, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD2D8Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned char uc, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD2D16Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned short us, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemsetD2D32Async(CUdeviceptr dstDevice, size_t dstPitch, unsigned int ui, size_t Width, size_t Height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuArrayCreate(CUarray* pHandle, const CUDA_ARRAY_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuArrayGetDescriptor(CUDA_ARRAY_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUarray array) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMipmappedArrayGetSparseProperties(CUDA_ARRAY_SPARSE_PROPERTIES* sparseProperties, CUmipmappedArray mipmap) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUarray array, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMipmappedArrayGetMemoryRequirements(CUDA_ARRAY_MEMORY_REQUIREMENTS* memoryRequirements, CUmipmappedArray mipmap, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuArrayGetPlane(CUarray* pPlaneArray, CUarray hArray, unsigned int planeIdx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuArrayDestroy(CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuArray3DCreate(CUarray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pAllocateArray) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuArray3DGetDescriptor(CUDA_ARRAY3D_DESCRIPTOR* pArrayDescriptor, CUarray hArray) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMipmappedArrayCreate(CUmipmappedArray* pHandle, const CUDA_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc, unsigned int numMipmapLevels) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMipmappedArrayGetLevel(CUarray* pLevelArray, CUmipmappedArray hMipmappedArray, unsigned int level) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMipmappedArrayDestroy(CUmipmappedArray hMipmappedArray) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemGetHandleForAddressRange(void* handle, CUdeviceptr dptr, size_t size, CUmemRangeHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemBatchDecompressAsync(CUmemDecompressParams* paramsArray, size_t count, unsigned int flags, size_t* errorIndex, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAddressReserve(CUdeviceptr* ptr, size_t size, size_t alignment, CUdeviceptr addr, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAddressFree(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemCreate(CUmemGenericAllocationHandle* handle, size_t size, const CUmemAllocationProp* prop, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemRelease(CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemMap(CUdeviceptr ptr, size_t size, size_t offset, CUmemGenericAllocationHandle handle, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemMapArrayAsync(CUarrayMapInfo* mapInfoList, unsigned int count, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemUnmap(CUdeviceptr ptr, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemSetAccess(CUdeviceptr ptr, size_t size, const CUmemAccessDesc* desc, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemGetAccess(unsigned long long* flags, const CUmemLocation* location, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemExportToShareableHandle(void* shareableHandle, CUmemGenericAllocationHandle handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemImportFromShareableHandle(CUmemGenericAllocationHandle* handle, void* osHandle, CUmemAllocationHandleType shHandleType) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemGetAllocationGranularity(size_t* granularity, const CUmemAllocationProp* prop, CUmemAllocationGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemGetAllocationPropertiesFromHandle(CUmemAllocationProp* prop, CUmemGenericAllocationHandle handle) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemRetainAllocationHandle(CUmemGenericAllocationHandle* handle, void* addr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemFreeAsync(CUdeviceptr dptr, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAllocAsync(CUdeviceptr* dptr, size_t bytesize, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolTrimTo(CUmemoryPool pool, size_t minBytesToKeep) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolSetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolGetAttribute(CUmemoryPool pool, CUmemPool_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolSetAccess(CUmemoryPool pool, const CUmemAccessDesc* map, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolGetAccess(CUmemAccess_flags* flags, CUmemoryPool memPool, CUmemLocation* location) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolCreate(CUmemoryPool* pool, const CUmemPoolProps* poolProps) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolDestroy(CUmemoryPool pool) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAllocFromPoolAsync(CUdeviceptr* dptr, size_t bytesize, CUmemoryPool pool, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolExportToShareableHandle(void* handle_out, CUmemoryPool pool, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolImportFromShareableHandle(CUmemoryPool* pool_out, void* handle, CUmemAllocationHandleType handleType, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolExportPointer(CUmemPoolPtrExportData* shareData_out, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPoolImportPointer(CUdeviceptr* ptr_out, CUmemoryPool pool, CUmemPoolPtrExportData* shareData) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMulticastCreate(CUmemGenericAllocationHandle* mcHandle, const CUmulticastObjectProp* prop) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMulticastAddDevice(CUmemGenericAllocationHandle mcHandle, CUdevice dev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef CUresult cuMulticastBindAddr(CUmemGenericAllocationHandle mcHandle, size_t mcOffset, CUdeviceptr memptr, size_t size, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMulticastUnbind(CUmemGenericAllocationHandle mcHandle, CUdevice dev, size_t mcOffset, size_t size) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMulticastGetGranularity(size_t* granularity, const CUmulticastObjectProp* prop, CUmulticastGranularity_flags option) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuPointerGetAttribute(void* data, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPrefetchAsync(CUdeviceptr devPtr, size_t count, CUdevice dstDevice, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemPrefetchAsync_v2(CUdeviceptr devPtr, size_t count, CUmemLocation location, unsigned int flags, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAdvise(CUdeviceptr devPtr, size_t count, CUmem_advise advice, CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemAdvise_v2(CUdeviceptr devPtr, size_t count, CUmem_advise advice, CUmemLocation location) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuMemRangeGetAttribute(void* data, size_t dataSize, CUmem_range_attribute attribute, CUdeviceptr devPtr, size_t count) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef CUresult cuPointerSetAttribute(const void* value, CUpointer_attribute attribute, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuPointerGetAttributes(unsigned int numAttributes, CUpointer_attribute* attributes, void** data, CUdeviceptr ptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamCreate(CUstream* phStream, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamCreateWithPriority(CUstream* phStream, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamGetPriority(CUstream hStream, int* priority) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamGetDevice(CUstream hStream, CUdevice* device) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamGetFlags(CUstream hStream, unsigned int* flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamGetId(CUstream hStream, unsigned long long* streamId) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamGetCtx(CUstream hStream, CUcontext* pctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamGetCtx_v2(CUstream hStream, CUcontext* pCtx, CUgreenCtx* pGreenCtx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamWaitEvent(CUstream hStream, CUevent hEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamAddCallback(CUstream hStream, CUstreamCallback callback, void* userData, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamBeginCapture(CUstream hStream, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamBeginCaptureToGraph(CUstream hStream, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUstreamCaptureMode mode) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuThreadExchangeStreamCaptureMode(CUstreamCaptureMode* mode) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamEndCapture(CUstream hStream, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamIsCapturing(CUstream hStream, CUstreamCaptureStatus* captureStatus) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamGetCaptureInfo(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
cdef CUresult cuStreamGetCaptureInfo_v3(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
cdef CUresult cuStreamUpdateCaptureDependencies(CUstream hStream, CUgraphNode* dependencies, size_t numDependencies, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamUpdateCaptureDependencies_v2(CUstream hStream, CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamAttachMemAsync(CUstream hStream, CUdeviceptr dptr, size_t length, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamQuery(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamSynchronize(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamDestroy(CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamCopyAttributes(CUstream dst, CUstream src) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamGetAttribute(CUstream hStream, CUstreamAttrID attr, CUstreamAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamSetAttribute(CUstream hStream, CUstreamAttrID attr, const CUstreamAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEventCreate(CUevent* phEvent, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEventRecord(CUevent hEvent, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEventRecordWithFlags(CUevent hEvent, CUstream hStream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEventQuery(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEventSynchronize(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEventDestroy(CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEventElapsedTime(float* pMilliseconds, CUevent hStart, CUevent hEnd) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEventElapsedTime_v2(float* pMilliseconds, CUevent hStart, CUevent hEnd) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuImportExternalMemory(CUexternalMemory* extMem_out, const CUDA_EXTERNAL_MEMORY_HANDLE_DESC* memHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuExternalMemoryGetMappedBuffer(CUdeviceptr* devPtr, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_BUFFER_DESC* bufferDesc) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuExternalMemoryGetMappedMipmappedArray(CUmipmappedArray* mipmap, CUexternalMemory extMem, const CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC* mipmapDesc) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDestroyExternalMemory(CUexternalMemory extMem) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuImportExternalSemaphore(CUexternalSemaphore* extSem_out, const CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC* semHandleDesc) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuSignalExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuWaitExternalSemaphoresAsync(const CUexternalSemaphore* extSemArray, const CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* paramsArray, unsigned int numExtSems, CUstream stream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDestroyExternalSemaphore(CUexternalSemaphore extSem) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamWaitValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamWaitValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamWriteValue32(CUstream stream, CUdeviceptr addr, cuuint32_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamWriteValue64(CUstream stream, CUdeviceptr addr, cuuint64_t value, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamBatchMemOp(CUstream stream, unsigned int count, CUstreamBatchMemOpParams* paramArray, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncGetAttribute(int* pi, CUfunction_attribute attrib, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncSetAttribute(CUfunction hfunc, CUfunction_attribute attrib, int value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncSetCacheConfig(CUfunction hfunc, CUfunc_cache config) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncGetModule(CUmodule* hmod, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncGetName(const char** name, CUfunction hfunc) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncGetParamInfo(CUfunction func, size_t paramIndex, size_t* paramOffset, size_t* paramSize) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncIsLoaded(CUfunctionLoadingState* state, CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncLoad(CUfunction function) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef CUresult cuLaunchKernelEx(const CUlaunchConfig* config, CUfunction f, void** kernelParams, void** extra) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef CUresult cuLaunchCooperativeKernelMultiDevice(CUDA_LAUNCH_PARAMS* launchParamsList, unsigned int numDevices, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLaunchHostFunc(CUstream hStream, CUhostFn fn, void* userData) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncSetBlockShape(CUfunction hfunc, int x, int y, int z) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncSetSharedSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuParamSetSize(CUfunction hfunc, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuParamSeti(CUfunction hfunc, int offset, unsigned int value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuParamSetf(CUfunction hfunc, int offset, float value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuParamSetv(CUfunction hfunc, int offset, void* ptr, unsigned int numbytes) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLaunch(CUfunction f) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLaunchGrid(CUfunction f, int grid_width, int grid_height) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLaunchGridAsync(CUfunction f, int grid_width, int grid_height, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuParamSetTexRef(CUfunction hfunc, int texunit, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuFuncSetSharedMemConfig(CUfunction hfunc, CUsharedconfig config) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphCreate(CUgraph* phGraph, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddKernelNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphKernelNodeGetParams(CUgraphNode hNode, CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphKernelNodeSetParams(CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddMemcpyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphMemcpyNodeGetParams(CUgraphNode hNode, CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphMemcpyNodeSetParams(CUgraphNode hNode, const CUDA_MEMCPY3D* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef CUresult cuGraphMemsetNodeGetParams(CUgraphNode hNode, CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphMemsetNodeSetParams(CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddHostNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphHostNodeGetParams(CUgraphNode hNode, CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphHostNodeSetParams(CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddChildGraphNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphChildGraphNodeGetGraph(CUgraphNode hNode, CUgraph* phGraph) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddEmptyNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddEventRecordNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphEventRecordNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphEventRecordNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddEventWaitNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphEventWaitNodeGetEvent(CUgraphNode hNode, CUevent* event_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphEventWaitNodeSetEvent(CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef CUresult cuGraphExternalSemaphoresSignalNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExternalSemaphoresSignalNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef CUresult cuGraphExternalSemaphoresWaitNodeGetParams(CUgraphNode hNode, CUDA_EXT_SEM_WAIT_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExternalSemaphoresWaitNodeSetParams(CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef CUresult cuGraphBatchMemOpNodeGetParams(CUgraphNode hNode, CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphBatchMemOpNodeSetParams(CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecBatchMemOpNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_BATCH_MEM_OP_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddMemAllocNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUDA_MEM_ALLOC_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphMemAllocNodeGetParams(CUgraphNode hNode, CUDA_MEM_ALLOC_NODE_PARAMS* params_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddMemFreeNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUdeviceptr dptr) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphMemFreeNodeGetParams(CUgraphNode hNode, CUdeviceptr* dptr_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGraphMemTrim(CUdevice device) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceSetGraphMemAttribute(CUdevice device, CUgraphMem_attribute attr, void* value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphClone(CUgraph* phGraphClone, CUgraph originalGraph) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphNodeFindInClone(CUgraphNode* phNode, CUgraphNode hOriginalNode, CUgraph hClonedGraph) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphNodeGetType(CUgraphNode hNode, CUgraphNodeType* typename) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphGetNodes(CUgraph hGraph, CUgraphNode* nodes, size_t* numNodes) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphGetRootNodes(CUgraph hGraph, CUgraphNode* rootNodes, size_t* numRootNodes) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphGetEdges(CUgraph hGraph, CUgraphNode* from_, CUgraphNode* to, size_t* numEdges) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphGetEdges_v2(CUgraph hGraph, CUgraphNode* from_, CUgraphNode* to, CUgraphEdgeData* edgeData, size_t* numEdges) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphNodeGetDependencies(CUgraphNode hNode, CUgraphNode* dependencies, size_t* numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphNodeGetDependencies_v2(CUgraphNode hNode, CUgraphNode* dependencies, CUgraphEdgeData* edgeData, size_t* numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphNodeGetDependentNodes(CUgraphNode hNode, CUgraphNode* dependentNodes, size_t* numDependentNodes) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphNodeGetDependentNodes_v2(CUgraphNode hNode, CUgraphNode* dependentNodes, CUgraphEdgeData* edgeData, size_t* numDependentNodes) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddDependencies_v2(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphRemoveDependencies(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphRemoveDependencies_v2(CUgraph hGraph, const CUgraphNode* from_, const CUgraphNode* to, const CUgraphEdgeData* edgeData, size_t numDependencies) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphDestroyNode(CUgraphNode hNode) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphInstantiate(CUgraphExec* phGraphExec, CUgraph hGraph, unsigned long long flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphInstantiateWithParams(CUgraphExec* phGraphExec, CUgraph hGraph, CUDA_GRAPH_INSTANTIATE_PARAMS* instantiateParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecGetFlags(CUgraphExec hGraphExec, cuuint64_t* flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecKernelNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_KERNEL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecMemcpyNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMCPY3D* copyParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecMemsetNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_MEMSET_NODE_PARAMS* memsetParams, CUcontext ctx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecHostNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_HOST_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecChildGraphNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraph childGraph) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecEventRecordNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecEventWaitNodeSetEvent(CUgraphExec hGraphExec, CUgraphNode hNode, CUevent event) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecExternalSemaphoresSignalNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_SIGNAL_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecExternalSemaphoresWaitNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, const CUDA_EXT_SEM_WAIT_NODE_PARAMS* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphNodeSetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphNodeGetEnabled(CUgraphExec hGraphExec, CUgraphNode hNode, unsigned int* isEnabled) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphUpload(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphLaunch(CUgraphExec hGraphExec, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecDestroy(CUgraphExec hGraphExec) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphDestroy(CUgraph hGraph) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecUpdate(CUgraphExec hGraphExec, CUgraph hGraph, CUgraphExecUpdateResultInfo* resultInfo) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphKernelNodeCopyAttributes(CUgraphNode dst, CUgraphNode src) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphKernelNodeGetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, CUkernelNodeAttrValue* value_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphKernelNodeSetAttribute(CUgraphNode hNode, CUkernelNodeAttrID attr, const CUkernelNodeAttrValue* value) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphDebugDotPrint(CUgraph hGraph, const char* path, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuUserObjectCreate(CUuserObject* object_out, void* ptr, CUhostFn destroy, unsigned int initialRefcount, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuUserObjectRetain(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuUserObjectRelease(CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphRetainUserObject(CUgraph graph, CUuserObject object, unsigned int count, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphReleaseUserObject(CUgraph graph, CUuserObject object, unsigned int count) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddNode(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, size_t numDependencies, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphAddNode_v2(CUgraphNode* phGraphNode, CUgraph hGraph, const CUgraphNode* dependencies, const CUgraphEdgeData* dependencyData, size_t numDependencies, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphNodeSetParams(CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphExecNodeSetParams(CUgraphExec hGraphExec, CUgraphNode hNode, CUgraphNodeParams* nodeParams) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphConditionalHandleCreate(CUgraphConditionalHandle* pHandle_out, CUgraph hGraph, CUcontext ctx, unsigned int defaultLaunchValue, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int* numBlocks, CUfunction func, int blockSize, size_t dynamicSMemSize, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuOccupancyMaxPotentialBlockSize(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuOccupancyMaxPotentialBlockSizeWithFlags(int* minGridSize, int* blockSize, CUfunction func, CUoccupancyB2DSize blockSizeToDynamicSMemSize, size_t dynamicSMemSize, int blockSizeLimit, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, CUfunction func, int numBlocks, int blockSize) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuOccupancyMaxPotentialClusterSize(int* clusterSize, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuOccupancyMaxActiveClusters(int* numClusters, CUfunction func, const CUlaunchConfig* config) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetArray(CUtexref hTexRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetMipmappedArray(CUtexref hTexRef, CUmipmappedArray hMipmappedArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetAddress(size_t* ByteOffset, CUtexref hTexRef, CUdeviceptr dptr, size_t numbytes) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetAddress2D(CUtexref hTexRef, const CUDA_ARRAY_DESCRIPTOR* desc, CUdeviceptr dptr, size_t Pitch) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetFormat(CUtexref hTexRef, CUarray_format fmt, int NumPackedComponents) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetAddressMode(CUtexref hTexRef, int dim, CUaddress_mode am) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetMipmapFilterMode(CUtexref hTexRef, CUfilter_mode fm) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetMipmapLevelBias(CUtexref hTexRef, float bias) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetMipmapLevelClamp(CUtexref hTexRef, float minMipmapLevelClamp, float maxMipmapLevelClamp) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetMaxAnisotropy(CUtexref hTexRef, unsigned int maxAniso) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetBorderColor(CUtexref hTexRef, float* pBorderColor) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefSetFlags(CUtexref hTexRef, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetAddress(CUdeviceptr* pdptr, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetArray(CUarray* phArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetMipmappedArray(CUmipmappedArray* phMipmappedArray, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetAddressMode(CUaddress_mode* pam, CUtexref hTexRef, int dim) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetFormat(CUarray_format* pFormat, int* pNumChannels, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetMipmapFilterMode(CUfilter_mode* pfm, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetMipmapLevelBias(float* pbias, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetMipmapLevelClamp(float* pminMipmapLevelClamp, float* pmaxMipmapLevelClamp, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetMaxAnisotropy(int* pmaxAniso, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetBorderColor(float* pBorderColor, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefGetFlags(unsigned int* pFlags, CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefCreate(CUtexref* pTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexRefDestroy(CUtexref hTexRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuSurfRefSetArray(CUsurfref hSurfRef, CUarray hArray, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuSurfRefGetArray(CUarray* phArray, CUsurfref hSurfRef) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef CUresult cuTexObjectDestroy(CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexObjectGetTextureDesc(CUDA_TEXTURE_DESC* pTexDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuTexObjectGetResourceViewDesc(CUDA_RESOURCE_VIEW_DESC* pResViewDesc, CUtexObject texObject) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuSurfObjectCreate(CUsurfObject* pSurfObject, const CUDA_RESOURCE_DESC* pResDesc) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuSurfObjectDestroy(CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuSurfObjectGetResourceDesc(CUDA_RESOURCE_DESC* pResDesc, CUsurfObject surfObject) except ?CUDA_ERROR_NOT_FOUND nogil
cdef 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
cdef 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
cdef 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
cdef CUresult cuTensorMapReplaceAddress(CUtensorMap* tensorMap, void* globalAddress) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceCanAccessPeer(int* canAccessPeer, CUdevice dev, CUdevice peerDev) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxEnablePeerAccess(CUcontext peerContext, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxDisablePeerAccess(CUcontext peerContext) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetP2PAttribute(int* value, CUdevice_P2PAttribute attrib, CUdevice srcDevice, CUdevice dstDevice) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsUnregisterResource(CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsSubResourceGetMappedArray(CUarray* pArray, CUgraphicsResource resource, unsigned int arrayIndex, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsResourceGetMappedMipmappedArray(CUmipmappedArray* pMipmappedArray, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsResourceGetMappedPointer(CUdeviceptr* pDevPtr, size_t* pSize, CUgraphicsResource resource) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsResourceSetMapFlags(CUgraphicsResource resource, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsMapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsUnmapResources(unsigned int count, CUgraphicsResource* resources, CUstream hStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGetProcAddress(const char* symbol, void** pfn, int cudaVersion, cuuint64_t flags, CUdriverProcAddressQueryResult* symbolStatus) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCoredumpGetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCoredumpGetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCoredumpSetAttribute(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCoredumpSetAttributeGlobal(CUcoredumpSettings attrib, void* value, size_t* size) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGetExportTable(const void** ppExportTable, const CUuuid* pExportTableId) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGreenCtxCreate(CUgreenCtx* phCtx, CUdevResourceDesc desc, CUdevice dev, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGreenCtxDestroy(CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxFromGreenCtx(CUcontext* pContext, CUgreenCtx hCtx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDeviceGetDevResource(CUdevice device, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCtxGetDevResource(CUcontext hCtx, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGreenCtxGetDevResource(CUgreenCtx hCtx, CUdevResource* resource, CUdevResourceType typename) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDevSmResourceSplitByCount(CUdevResource* result, unsigned int* nbGroups, const CUdevResource* input, CUdevResource* remaining, unsigned int useFlags, unsigned int minCount) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuDevResourceGenerateDesc(CUdevResourceDesc* phDesc, CUdevResource* resources, unsigned int nbResources) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGreenCtxRecordEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGreenCtxWaitEvent(CUgreenCtx hCtx, CUevent hEvent) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuStreamGetGreenCtx(CUstream hStream, CUgreenCtx* phCtx) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGreenCtxStreamCreate(CUstream* phStream, CUgreenCtx greenCtx, unsigned int flags, int priority) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLogsRegisterCallback(CUlogsCallback callbackFunc, void* userData, CUlogsCallbackHandle* callback_out) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLogsUnregisterCallback(CUlogsCallbackHandle callback) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLogsCurrent(CUlogIterator* iterator_out, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLogsDumpToFile(CUlogIterator* iterator, const char* pathToFile, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuLogsDumpToMemory(CUlogIterator* iterator, char* buffer, size_t* size, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCheckpointProcessGetRestoreThreadId(int pid, int* tid) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCheckpointProcessGetState(int pid, CUprocessState* state) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCheckpointProcessLock(int pid, CUcheckpointLockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCheckpointProcessCheckpoint(int pid, CUcheckpointCheckpointArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCheckpointProcessRestore(int pid, CUcheckpointRestoreArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuCheckpointProcessUnlock(int pid, CUcheckpointUnlockArgs* args) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuProfilerStart() except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuProfilerStop() except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsEGLRegisterImage(CUgraphicsResource* pCudaResource, EGLImageKHR image, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEGLStreamConsumerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEGLStreamConsumerConnectWithFlags(CUeglStreamConnection* conn, EGLStreamKHR stream, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEGLStreamConsumerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEGLStreamConsumerAcquireFrame(CUeglStreamConnection* conn, CUgraphicsResource* pCudaResource, CUstream* pStream, unsigned int timeout) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEGLStreamConsumerReleaseFrame(CUeglStreamConnection* conn, CUgraphicsResource pCudaResource, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEGLStreamProducerConnect(CUeglStreamConnection* conn, EGLStreamKHR stream, EGLint width, EGLint height) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEGLStreamProducerDisconnect(CUeglStreamConnection* conn) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEGLStreamProducerPresentFrame(CUeglStreamConnection* conn, CUeglFrame eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEGLStreamProducerReturnFrame(CUeglStreamConnection* conn, CUeglFrame* eglframe, CUstream* pStream) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsResourceGetMappedEglFrame(CUeglFrame* eglFrame, CUgraphicsResource resource, unsigned int index, unsigned int mipLevel) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuEventCreateFromEGLSync(CUevent* phEvent, EGLSyncKHR eglSync, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsGLRegisterBuffer(CUgraphicsResource* pCudaResource, GLuint buffer, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsGLRegisterImage(CUgraphicsResource* pCudaResource, GLuint image, GLenum target, unsigned int Flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGLGetDevices(unsigned int* pCudaDeviceCount, CUdevice* pCudaDevices, unsigned int cudaDeviceCount, CUGLDeviceList deviceList) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuVDPAUGetDevice(CUdevice* pDevice, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuVDPAUCtxCreate(CUcontext* pCtx, unsigned int flags, CUdevice device, VdpDevice vdpDevice, VdpGetProcAddress* vdpGetProcAddress) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsVDPAURegisterVideoSurface(CUgraphicsResource* pCudaResource, VdpVideoSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef CUresult cuGraphicsVDPAURegisterOutputSurface(CUgraphicsResource* pCudaResource, VdpOutputSurface vdpSurface, unsigned int flags) except ?CUDA_ERROR_NOT_FOUND nogil
cdef enum: CUDA_VERSION = 12090
cdef enum: CU_IPC_HANDLE_SIZE = 64
cdef enum: CU_STREAM_LEGACY = 1
cdef enum: CU_STREAM_PER_THREAD = 2
cdef enum: CU_COMPUTE_ACCELERATED_TARGET_BASE = 65536
cdef enum: CU_COMPUTE_FAMILY_TARGET_BASE = 131072
cdef enum: CU_GRAPH_COND_ASSIGN_DEFAULT = 1
cdef enum: CU_GRAPH_KERNEL_NODE_PORT_DEFAULT = 0
cdef enum: CU_GRAPH_KERNEL_NODE_PORT_PROGRAMMATIC = 1
cdef enum: CU_GRAPH_KERNEL_NODE_PORT_LAUNCH_ORDER = 2
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_ACCESS_POLICY_WINDOW = 1
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_COOPERATIVE = 2
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_CLUSTER_DIMENSION = 4
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_CLUSTER_SCHEDULING_POLICY_PREFERENCE = 5
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_PRIORITY = 8
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_MEM_SYNC_DOMAIN_MAP = 9
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_MEM_SYNC_DOMAIN = 10
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_PREFERRED_CLUSTER_DIMENSION = 11
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_DEVICE_UPDATABLE_KERNEL_NODE = 13
cdef enum: CU_KERNEL_NODE_ATTRIBUTE_PREFERRED_SHARED_MEMORY_CARVEOUT = 14
cdef enum: CU_STREAM_ATTRIBUTE_ACCESS_POLICY_WINDOW = 1
cdef enum: CU_STREAM_ATTRIBUTE_SYNCHRONIZATION_POLICY = 3
cdef enum: CU_STREAM_ATTRIBUTE_PRIORITY = 8
cdef enum: CU_STREAM_ATTRIBUTE_MEM_SYNC_DOMAIN_MAP = 9
cdef enum: CU_STREAM_ATTRIBUTE_MEM_SYNC_DOMAIN = 10
cdef enum: CU_MEMHOSTALLOC_PORTABLE = 1
cdef enum: CU_MEMHOSTALLOC_DEVICEMAP = 2
cdef enum: CU_MEMHOSTALLOC_WRITECOMBINED = 4
cdef enum: CU_MEMHOSTREGISTER_PORTABLE = 1
cdef enum: CU_MEMHOSTREGISTER_DEVICEMAP = 2
cdef enum: CU_MEMHOSTREGISTER_IOMEMORY = 4
cdef enum: CU_MEMHOSTREGISTER_READ_ONLY = 8
cdef enum: CU_ARRAY_SPARSE_PROPERTIES_SINGLE_MIPTAIL = 1
cdef enum: CU_TENSOR_MAP_NUM_QWORDS = 16
cdef enum: CUDA_EXTERNAL_MEMORY_DEDICATED = 1
cdef enum: CUDA_EXTERNAL_SEMAPHORE_SIGNAL_SKIP_NVSCIBUF_MEMSYNC = 1
cdef enum: CUDA_EXTERNAL_SEMAPHORE_WAIT_SKIP_NVSCIBUF_MEMSYNC = 2
cdef enum: CUDA_NVSCISYNC_ATTR_SIGNAL = 1
cdef enum: CUDA_NVSCISYNC_ATTR_WAIT = 2
cdef enum: CU_MEM_CREATE_USAGE_TILE_POOL = 1
cdef enum: CU_MEM_CREATE_USAGE_HW_DECOMPRESS = 2
cdef enum: CU_MEM_POOL_CREATE_USAGE_HW_DECOMPRESS = 2
cdef enum: CUDA_COOPERATIVE_LAUNCH_MULTI_DEVICE_NO_PRE_LAUNCH_SYNC = 1
cdef enum: CUDA_COOPERATIVE_LAUNCH_MULTI_DEVICE_NO_POST_LAUNCH_SYNC = 2
cdef enum: CUDA_ARRAY3D_LAYERED = 1
cdef enum: CUDA_ARRAY3D_2DARRAY = 1
cdef enum: CUDA_ARRAY3D_SURFACE_LDST = 2
cdef enum: CUDA_ARRAY3D_CUBEMAP = 4
cdef enum: CUDA_ARRAY3D_TEXTURE_GATHER = 8
cdef enum: CUDA_ARRAY3D_DEPTH_TEXTURE = 16
cdef enum: CUDA_ARRAY3D_COLOR_ATTACHMENT = 32
cdef enum: CUDA_ARRAY3D_SPARSE = 64
cdef enum: CUDA_ARRAY3D_DEFERRED_MAPPING = 128
cdef enum: CUDA_ARRAY3D_VIDEO_ENCODE_DECODE = 256
cdef enum: CU_TRSA_OVERRIDE_FORMAT = 1
cdef enum: CU_TRSF_READ_AS_INTEGER = 1
cdef enum: CU_TRSF_NORMALIZED_COORDINATES = 2
cdef enum: CU_TRSF_SRGB = 16
cdef enum: CU_TRSF_DISABLE_TRILINEAR_OPTIMIZATION = 32
cdef enum: CU_TRSF_SEAMLESS_CUBEMAP = 64
cdef enum: CU_LAUNCH_KERNEL_REQUIRED_BLOCK_DIM = 1
cdef enum: CU_LAUNCH_PARAM_END_AS_INT = 0
cdef enum: CU_LAUNCH_PARAM_END = 0
cdef enum: CU_LAUNCH_PARAM_BUFFER_POINTER_AS_INT = 1
cdef enum: CU_LAUNCH_PARAM_BUFFER_POINTER = 1
cdef enum: CU_LAUNCH_PARAM_BUFFER_SIZE_AS_INT = 2
cdef enum: CU_LAUNCH_PARAM_BUFFER_SIZE = 2
cdef enum: CU_PARAM_TR_DEFAULT = -1
cdef enum: CU_DEVICE_CPU = -1
cdef enum: CU_DEVICE_INVALID = -2
cdef enum: RESOURCE_ABI_VERSION = 1
cdef enum: RESOURCE_ABI_EXTERNAL_BYTES = 48
cdef enum: MAX_PLANES = 3
cdef enum: CUDA_EGL_INFINITE_TIMEOUT = 4294967295 |