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
|
/* ************************************************************************
* Copyright (C) 2018-2022 Advanced Micro Devices, Inc. All rights Reserved.
*
* Permission is hereby granted, free of charge, to any person obtaining a copy
* of this software and associated documentation files (the "Software"), to deal
* in the Software without restriction, including without limitation the rights
* to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
* copies of the Software, and to permit persons to whom the Software is
* furnished to do so, subject to the following conditions:
*
* The above copyright notice and this permission notice shall be included in
* all copies or substantial portions of the Software.
*
* THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
* IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
* FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
* AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
* LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
* OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
* THE SOFTWARE.
*
* ************************************************************************ */
/*! \file
* \brief rocsparse-auxiliary.h provides auxilary functions in rocsparse
*/
#ifndef _ROCSPARSE_AUXILIARY_H_
#define _ROCSPARSE_AUXILIARY_H_
#include "rocsparse-export.h"
#include "rocsparse-types.h"
#ifdef __cplusplus
extern "C" {
#endif
/*! \ingroup aux_module
* \brief Create a rocsparse handle
*
* \details
* \p rocsparse_create_handle creates the rocSPARSE library context. It must be
* initialized before any other rocSPARSE API function is invoked and must be passed to
* all subsequent library function calls. The handle should be destroyed at the end
* using rocsparse_destroy_handle().
*
* @param[out]
* handle the pointer to the handle to the rocSPARSE library context.
*
* \retval rocsparse_status_success the initialization succeeded.
* \retval rocsparse_status_invalid_handle \p handle pointer is invalid.
* \retval rocsparse_status_internal_error an internal error occurred.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_handle(rocsparse_handle* handle);
/*! \ingroup aux_module
* \brief Destroy a rocsparse handle
*
* \details
* \p rocsparse_destroy_handle destroys the rocSPARSE library context and releases all
* resources used by the rocSPARSE library.
*
* @param[in]
* handle the handle to the rocSPARSE library context.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_handle \p handle is invalid.
* \retval rocsparse_status_internal_error an internal error occurred.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_destroy_handle(rocsparse_handle handle);
/*! \ingroup aux_module
* \brief Specify user defined HIP stream
*
* \details
* \p rocsparse_set_stream specifies the stream to be used by the rocSPARSE library
* context and all subsequent function calls.
*
* @param[inout]
* handle the handle to the rocSPARSE library context.
* @param[in]
* stream the stream to be used by the rocSPARSE library context.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_handle \p handle is invalid.
*
* \par Example
* This example illustrates, how a user defined stream can be used in rocSPARSE.
* \code{.c}
* // Create rocSPARSE handle
* rocsparse_handle handle;
* rocsparse_create_handle(&handle);
*
* // Create stream
* hipStream_t stream;
* hipStreamCreate(&stream);
*
* // Set stream to rocSPARSE handle
* rocsparse_set_stream(handle, stream);
*
* // Do some work
* // ...
*
* // Clean up
* rocsparse_destroy_handle(handle);
* hipStreamDestroy(stream);
* \endcode
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_set_stream(rocsparse_handle handle, hipStream_t stream);
/*! \ingroup aux_module
* \brief Get current stream from library context
*
* \details
* \p rocsparse_get_stream gets the rocSPARSE library context stream which is currently
* used for all subsequent function calls.
*
* @param[in]
* handle the handle to the rocSPARSE library context.
* @param[out]
* stream the stream currently used by the rocSPARSE library context.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_handle \p handle is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_get_stream(rocsparse_handle handle, hipStream_t* stream);
/*! \ingroup aux_module
* \brief Specify pointer mode
*
* \details
* \p rocsparse_set_pointer_mode specifies the pointer mode to be used by the rocSPARSE
* library context and all subsequent function calls. By default, all values are passed
* by reference on the host. Valid pointer modes are \ref rocsparse_pointer_mode_host
* or \p rocsparse_pointer_mode_device.
*
* @param[in]
* handle the handle to the rocSPARSE library context.
* @param[in]
* pointer_mode the pointer mode to be used by the rocSPARSE library context.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_handle \p handle is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_set_pointer_mode(rocsparse_handle handle,
rocsparse_pointer_mode pointer_mode);
/*! \ingroup aux_module
* \brief Get current pointer mode from library context
*
* \details
* \p rocsparse_get_pointer_mode gets the rocSPARSE library context pointer mode which
* is currently used for all subsequent function calls.
*
* @param[in]
* handle the handle to the rocSPARSE library context.
* @param[out]
* pointer_mode the pointer mode that is currently used by the rocSPARSE library
* context.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_handle \p handle is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_get_pointer_mode(rocsparse_handle handle,
rocsparse_pointer_mode* pointer_mode);
/*! \ingroup aux_module
* \brief Get rocSPARSE version
*
* \details
* \p rocsparse_get_version gets the rocSPARSE library version number.
* - patch = version % 100
* - minor = version / 100 % 1000
* - major = version / 100000
*
* @param[in]
* handle the handle to the rocSPARSE library context.
* @param[out]
* version the version number of the rocSPARSE library.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_handle \p handle is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_get_version(rocsparse_handle handle, int* version);
/*! \ingroup aux_module
* \brief Get rocSPARSE git revision
*
* \details
* \p rocsparse_get_git_rev gets the rocSPARSE library git commit revision (SHA-1).
*
* @param[in]
* handle the handle to the rocSPARSE library context.
* @param[out]
* rev the git commit revision (SHA-1).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_handle \p handle is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_get_git_rev(rocsparse_handle handle, char* rev);
/*! \ingroup aux_module
* \brief Create a matrix descriptor
* \details
* \p rocsparse_create_mat_descr creates a matrix descriptor. It initializes
* \ref rocsparse_matrix_type to \ref rocsparse_matrix_type_general and
* \ref rocsparse_index_base to \ref rocsparse_index_base_zero. It should be destroyed
* at the end using rocsparse_destroy_mat_descr().
*
* @param[out]
* descr the pointer to the matrix descriptor.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr pointer is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_mat_descr(rocsparse_mat_descr* descr);
/*! \ingroup aux_module
* \brief Copy a matrix descriptor
* \details
* \p rocsparse_copy_mat_descr copies a matrix descriptor. Both, source and destination
* matrix descriptors must be initialized prior to calling \p rocsparse_copy_mat_descr.
*
* @param[out]
* dest the pointer to the destination matrix descriptor.
* @param[in]
* src the pointer to the source matrix descriptor.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p src or \p dest pointer is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_copy_mat_descr(rocsparse_mat_descr dest, const rocsparse_mat_descr src);
/*! \ingroup aux_module
* \brief Destroy a matrix descriptor
*
* \details
* \p rocsparse_destroy_mat_descr destroys a matrix descriptor and releases all
* resources used by the descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_destroy_mat_descr(rocsparse_mat_descr descr);
/*! \ingroup aux_module
* \brief Specify the index base of a matrix descriptor
*
* \details
* \p rocsparse_set_mat_index_base sets the index base of a matrix descriptor. Valid
* options are \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
*
* @param[inout]
* descr the matrix descriptor.
* @param[in]
* base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr pointer is invalid.
* \retval rocsparse_status_invalid_value \p base is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_set_mat_index_base(rocsparse_mat_descr descr, rocsparse_index_base base);
/*! \ingroup aux_module
* \brief Get the index base of a matrix descriptor
*
* \details
* \p rocsparse_get_mat_index_base returns the index base of a matrix descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \returns \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
*/
ROCSPARSE_EXPORT
rocsparse_index_base rocsparse_get_mat_index_base(const rocsparse_mat_descr descr);
/*! \ingroup aux_module
* \brief Specify the matrix type of a matrix descriptor
*
* \details
* \p rocsparse_set_mat_type sets the matrix type of a matrix descriptor. Valid
* matrix types are \ref rocsparse_matrix_type_general,
* \ref rocsparse_matrix_type_symmetric, \ref rocsparse_matrix_type_hermitian or
* \ref rocsparse_matrix_type_triangular.
*
* @param[inout]
* descr the matrix descriptor.
* @param[in]
* type \ref rocsparse_matrix_type_general, \ref rocsparse_matrix_type_symmetric,
* \ref rocsparse_matrix_type_hermitian or
* \ref rocsparse_matrix_type_triangular.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr pointer is invalid.
* \retval rocsparse_status_invalid_value \p type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_set_mat_type(rocsparse_mat_descr descr, rocsparse_matrix_type type);
/*! \ingroup aux_module
* \brief Get the matrix type of a matrix descriptor
*
* \details
* \p rocsparse_get_mat_type returns the matrix type of a matrix descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \returns \ref rocsparse_matrix_type_general, \ref rocsparse_matrix_type_symmetric,
* \ref rocsparse_matrix_type_hermitian or
* \ref rocsparse_matrix_type_triangular.
*/
ROCSPARSE_EXPORT
rocsparse_matrix_type rocsparse_get_mat_type(const rocsparse_mat_descr descr);
/*! \ingroup aux_module
* \brief Specify the matrix fill mode of a matrix descriptor
*
* \details
* \p rocsparse_set_mat_fill_mode sets the matrix fill mode of a matrix descriptor.
* Valid fill modes are \ref rocsparse_fill_mode_lower or
* \ref rocsparse_fill_mode_upper.
*
* @param[inout]
* descr the matrix descriptor.
* @param[in]
* fill_mode \ref rocsparse_fill_mode_lower or \ref rocsparse_fill_mode_upper.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr pointer is invalid.
* \retval rocsparse_status_invalid_value \p fill_mode is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_set_mat_fill_mode(rocsparse_mat_descr descr,
rocsparse_fill_mode fill_mode);
/*! \ingroup aux_module
* \brief Get the matrix fill mode of a matrix descriptor
*
* \details
* \p rocsparse_get_mat_fill_mode returns the matrix fill mode of a matrix descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \returns \ref rocsparse_fill_mode_lower or \ref rocsparse_fill_mode_upper.
*/
ROCSPARSE_EXPORT
rocsparse_fill_mode rocsparse_get_mat_fill_mode(const rocsparse_mat_descr descr);
/*! \ingroup aux_module
* \brief Specify the matrix diagonal type of a matrix descriptor
*
* \details
* \p rocsparse_set_mat_diag_type sets the matrix diagonal type of a matrix
* descriptor. Valid diagonal types are \ref rocsparse_diag_type_unit or
* \ref rocsparse_diag_type_non_unit.
*
* @param[inout]
* descr the matrix descriptor.
* @param[in]
* diag_type \ref rocsparse_diag_type_unit or \ref rocsparse_diag_type_non_unit.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr pointer is invalid.
* \retval rocsparse_status_invalid_value \p diag_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_set_mat_diag_type(rocsparse_mat_descr descr,
rocsparse_diag_type diag_type);
/*! \ingroup aux_module
* \brief Get the matrix diagonal type of a matrix descriptor
*
* \details
* \p rocsparse_get_mat_diag_type returns the matrix diagonal type of a matrix
* descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \returns \ref rocsparse_diag_type_unit or \ref rocsparse_diag_type_non_unit.
*/
ROCSPARSE_EXPORT
rocsparse_diag_type rocsparse_get_mat_diag_type(const rocsparse_mat_descr descr);
/*! \ingroup aux_module
* \brief Specify the matrix storage mode of a matrix descriptor
*
* \details
* \p rocsparse_set_mat_storage_mode sets the matrix storage mode of a matrix descriptor.
* Valid fill modes are \ref rocsparse_storage_mode_sorted or
* \ref rocsparse_storage_mode_unsorted.
*
* @param[inout]
* descr the matrix descriptor.
* @param[in]
* storage_mode \ref rocsparse_storage_mode_sorted or
* \ref rocsparse_storage_mode_unsorted.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr pointer is invalid.
* \retval rocsparse_status_invalid_value \p storage_mode is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_set_mat_storage_mode(rocsparse_mat_descr descr,
rocsparse_storage_mode storage_mode);
/*! \ingroup aux_module
* \brief Get the matrix storage mode of a matrix descriptor
*
* \details
* \p rocsparse_get_mat_storage_mode returns the matrix storage mode of a matrix descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \returns \ref rocsparse_storage_mode_sorted or \ref rocsparse_storage_mode_unsorted.
*/
ROCSPARSE_EXPORT
rocsparse_storage_mode rocsparse_get_mat_storage_mode(const rocsparse_mat_descr descr);
/*! \ingroup aux_module
* \brief Create a \p HYB matrix structure
*
* \details
* \p rocsparse_create_hyb_mat creates a structure that holds the matrix in \p HYB
* storage format. It should be destroyed at the end using rocsparse_destroy_hyb_mat().
*
* @param[inout]
* hyb the pointer to the hybrid matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p hyb pointer is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_hyb_mat(rocsparse_hyb_mat* hyb);
/*! \ingroup aux_module
* \brief Copy a \p HYB matrix structure
*
* \details
* \p rocsparse_copy_hyb_mat copies a matrix info structure. Both, source and destination
* matrix info structure must be initialized prior to calling \p rocsparse_copy_hyb_mat.
*
* @param[out]
* dest the pointer to the destination matrix info structure.
* @param[in]
* src the pointer to the source matrix info structure.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p hyb pointer is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_copy_hyb_mat(rocsparse_hyb_mat dest, const rocsparse_hyb_mat src);
/*! \ingroup aux_module
* \brief Destroy a \p HYB matrix structure
*
* \details
* \p rocsparse_destroy_hyb_mat destroys a \p HYB structure.
*
* @param[in]
* hyb the hybrid matrix structure.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p hyb pointer is invalid.
* \retval rocsparse_status_internal_error an internal error occurred.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_destroy_hyb_mat(rocsparse_hyb_mat hyb);
/*! \ingroup aux_module
* \brief Create a matrix info structure
*
* \details
* \p rocsparse_create_mat_info creates a structure that holds the matrix info data
* that is gathered during the analysis routines available. It should be destroyed
* at the end using rocsparse_destroy_mat_info().
*
* @param[inout]
* info the pointer to the info structure.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p info pointer is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_mat_info(rocsparse_mat_info* info);
/*! \ingroup aux_module
* \brief Copy a matrix info structure
* \details
* \p rocsparse_copy_mat_info copies a matrix info structure. Both, source and destination
* matrix info structure must be initialized prior to calling \p rocsparse_copy_mat_info.
*
* @param[out]
* dest the pointer to the destination matrix info structure.
* @param[in]
* src the pointer to the source matrix info structure.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p src or \p dest pointer is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_copy_mat_info(rocsparse_mat_info dest, const rocsparse_mat_info src);
/*! \ingroup aux_module
* \brief Destroy a matrix info structure
*
* \details
* \p rocsparse_destroy_mat_info destroys a matrix info structure.
*
* @param[in]
* info the info structure.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p info pointer is invalid.
* \retval rocsparse_status_internal_error an internal error occurred.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_destroy_mat_info(rocsparse_mat_info info);
/*! \ingroup aux_module
* \brief Create a color info structure
*
* \details
* \p rocsparse_create_color_info creates a structure that holds the color info data
* that is gathered during the analysis routines available. It should be destroyed
* at the end using rocsparse_destroy_color_info().
*
* @param[inout]
* info the pointer to the info structure.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p info pointer is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_color_info(rocsparse_color_info* info);
/*! \ingroup aux_module
* \brief Copy a color info structure
* \details
* \p rocsparse_copy_color_info copies a color info structure. Both, source and destination
* color info structure must be initialized prior to calling \p rocsparse_copy_color_info.
*
* @param[out]
* dest the pointer to the destination color info structure.
* @param[in]
* src the pointer to the source color info structure.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p src or \p dest pointer is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_copy_color_info(rocsparse_color_info dest,
const rocsparse_color_info src);
/*! \ingroup aux_module
* \brief Destroy a color info structure
*
* \details
* \p rocsparse_destroy_color_info destroys a color info structure.
*
* @param[in]
* info the info structure.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p info pointer is invalid.
* \retval rocsparse_status_internal_error an internal error occurred.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_destroy_color_info(rocsparse_color_info info);
// Generic API
/*! \ingroup aux_module
* \brief Create a sparse vector descriptor
* \details
* \p rocsparse_create_spvec_descr creates a sparse vector descriptor. It should be
* destroyed at the end using rocsparse_destroy_mat_descr().
*
* @param[out]
* descr the pointer to the sparse vector descriptor.
* @param[in]
* size size of the sparse vector.
* @param[in]
* nnz number of non-zeros in sparse vector.
* @param[in]
* indices indices of the sparse vector where non-zeros occur (must be array of length \p nnz ).
* @param[in]
* values non-zero values in the sparse vector (must be array of length \p nnz ).
* @param[in]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p indices or \p values is invalid.
* \retval rocsparse_status_invalid_size if \p size or \p nnz is invalid.
* \retval rocsparse_status_invalid_value if \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_spvec_descr(rocsparse_spvec_descr* descr,
int64_t size,
int64_t nnz,
void* indices,
void* values,
rocsparse_indextype idx_type,
rocsparse_index_base idx_base,
rocsparse_datatype data_type);
/*! \ingroup aux_module
* \brief Destroy a sparse vector descriptor
*
* \details
* \p rocsparse_destroy_spvec_descr destroys a sparse vector descriptor and releases all
* resources used by the descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_destroy_spvec_descr(rocsparse_spvec_descr descr);
/*! \ingroup aux_module
* \brief Get the fields of the sparse vector descriptor
* \details
* \p rocsparse_spvec_get gets the fields of the sparse vector descriptor
*
* @param[in]
* descr the pointer to the sparse vector descriptor.
* @param[out]
* size size of the sparse vector.
* @param[out]
* nnz number of non-zeros in sparse vector.
* @param[out]
* indices indices of the sparse vector where non-zeros occur (must be array of length \p nnz ).
* @param[out]
* values non-zero values in the sparse vector (must be array of length \p nnz ).
* @param[out]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[out]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[out]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p indices or \p values is invalid.
* \retval rocsparse_status_invalid_size if \p size or \p nnz is invalid.
* \retval rocsparse_status_invalid_value if \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spvec_get(const rocsparse_spvec_descr descr,
int64_t* size,
int64_t* nnz,
void** indices,
void** values,
rocsparse_indextype* idx_type,
rocsparse_index_base* idx_base,
rocsparse_datatype* data_type);
/*! \ingroup aux_module
* \brief Get the index base stored in the sparse vector descriptor
*
* @param[in]
* descr the pointer to the sparse vector descriptor.
* @param[out]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_value if \p idx_base is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spvec_get_index_base(const rocsparse_spvec_descr descr,
rocsparse_index_base* idx_base);
/*! \ingroup aux_module
* \brief Get the values array stored in the sparse vector descriptor
*
* @param[in]
* descr the pointer to the sparse vector descriptor.
* @param[out]
* values non-zero values in the sparse vector (must be array of length \p nnz ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p values is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spvec_get_values(const rocsparse_spvec_descr descr, void** values);
/*! \ingroup aux_module
* \brief Set the values array in the sparse vector descriptor
*
* @param[inout]
* descr the pointer to the sparse vector descriptor.
* @param[in]
* values non-zero values in the sparse vector (must be array of length \p nnz ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p values is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spvec_set_values(rocsparse_spvec_descr descr, void* values);
/*! \ingroup aux_module
* \brief Create a sparse COO matrix descriptor
* \details
* \p rocsparse_create_coo_descr creates a sparse COO matrix descriptor. It should be
* destroyed at the end using \p rocsparse_destroy_spmat_descr.
*
* @param[out]
* descr the pointer to the sparse COO matrix descriptor.
* @param[in]
* rows number of rows in the COO matrix.
* @param[in]
* cols number of columns in the COO matrix
* @param[in]
* nnz number of non-zeros in the COO matrix.
* @param[in]
* coo_row_ind row indices of the COO matrix (must be array of length \p nnz ).
* @param[in]
* coo_col_ind column indices of the COO matrix (must be array of length \p nnz ).
* @param[in]
* coo_val values of the COO matrix (must be array of length \p nnz ).
* @param[in]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p coo_row_ind or \p coo_col_ind or \p coo_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p nnz is invalid.
* \retval rocsparse_status_invalid_value if \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_coo_descr(rocsparse_spmat_descr* descr,
int64_t rows,
int64_t cols,
int64_t nnz,
void* coo_row_ind,
void* coo_col_ind,
void* coo_val,
rocsparse_indextype idx_type,
rocsparse_index_base idx_base,
rocsparse_datatype data_type);
/*! \ingroup aux_module
* \brief Create a sparse COO AoS matrix descriptor
* \details
* \p rocsparse_create_coo_aos_descr creates a sparse COO AoS matrix descriptor. It should be
* destroyed at the end using \p rocsparse_destroy_spmat_descr.
*
* @param[out]
* descr the pointer to the sparse COO AoS matrix descriptor.
* @param[in]
* rows number of rows in the COO AoS matrix.
* @param[in]
* cols number of columns in the COO AoS matrix
* @param[in]
* nnz number of non-zeros in the COO AoS matrix.
* @param[in]
* coo_ind <row, column> indices of the COO AoS matrix (must be array of length \p nnz ).
* @param[in]
* coo_val values of the COO AoS matrix (must be array of length \p nnz ).
* @param[in]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p coo_ind or \p coo_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p nnz is invalid.
* \retval rocsparse_status_invalid_value if \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_coo_aos_descr(rocsparse_spmat_descr* descr,
int64_t rows,
int64_t cols,
int64_t nnz,
void* coo_ind,
void* coo_val,
rocsparse_indextype idx_type,
rocsparse_index_base idx_base,
rocsparse_datatype data_type);
/*! \ingroup aux_module
* \brief Create a sparse BSR matrix descriptor
* \details
* \p rocsparse_create_bsr_descr creates a sparse BSR matrix descriptor. It should be
* destroyed at the end using \p rocsparse_destroy_spmat_descr.
*
* @param[out]
* descr the pointer to the sparse BSR matrix descriptor.
* @param[in]
* mb number of rows in the BSR matrix.
* @param[in]
* nb number of columns in the BSR matrix
* @param[in]
* nnzb number of non-zeros in the BSR matrix.
* @param[in]
* block_dir direction of the internal block storage.
* @param[in]
* block_dim dimension of the blocks.
* @param[in]
* bsr_row_ptr row offsets of the BSR matrix (must be array of length \p mb+1 ).
* @param[in]
* bsr_col_ind column indices of the BSR matrix (must be array of length \p nnzb ).
* @param[in]
* bsr_val values of the BSR matrix (must be array of length \p nnzb * \p block_dim * \p block_dim ).
* @param[in]
* row_ptr_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* col_ind_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p bsr_row_ptr or \p bsr_col_ind or \p bsr_val is invalid.
* \retval rocsparse_status_invalid_size if \p mb or \p nb or \p nnzb \p block_dim is invalid.
* \retval rocsparse_status_invalid_value if \p row_ptr_type or \p col_ind_type or \p idx_base or \p data_type or \p block_dir is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_bsr_descr(rocsparse_spmat_descr* descr,
int64_t mb,
int64_t nb,
int64_t nnzb,
rocsparse_direction block_dir,
int64_t block_dim,
void* bsr_row_ptr,
void* bsr_col_ind,
void* bsr_val,
rocsparse_indextype row_ptr_type,
rocsparse_indextype col_ind_type,
rocsparse_index_base idx_base,
rocsparse_datatype data_type);
/*! \ingroup aux_module
* \brief Create a sparse CSR matrix descriptor
* \details
* \p rocsparse_create_csr_descr creates a sparse CSR matrix descriptor. It should be
* destroyed at the end using \p rocsparse_destroy_spmat_descr.
*
* @param[out]
* descr the pointer to the sparse CSR matrix descriptor.
* @param[in]
* rows number of rows in the CSR matrix.
* @param[in]
* cols number of columns in the CSR matrix
* @param[in]
* nnz number of non-zeros in the CSR matrix.
* @param[in]
* csr_row_ptr row offsets of the CSR matrix (must be array of length \p rows+1 ).
* @param[in]
* csr_col_ind column indices of the CSR matrix (must be array of length \p nnz ).
* @param[in]
* csr_val values of the CSR matrix (must be array of length \p nnz ).
* @param[in]
* row_ptr_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* col_ind_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p csr_row_ptr or \p csr_col_ind or \p csr_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p nnz is invalid.
* \retval rocsparse_status_invalid_value if \p row_ptr_type or \p col_ind_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_csr_descr(rocsparse_spmat_descr* descr,
int64_t rows,
int64_t cols,
int64_t nnz,
void* csr_row_ptr,
void* csr_col_ind,
void* csr_val,
rocsparse_indextype row_ptr_type,
rocsparse_indextype col_ind_type,
rocsparse_index_base idx_base,
rocsparse_datatype data_type);
/*! \ingroup aux_module
* \brief Create a sparse CSC matrix descriptor
* \details
* \p rocsparse_create_csc_descr creates a sparse CSC matrix descriptor. It should be
* destroyed at the end using \p rocsparse_destroy_spmat_descr.
*
* @param[out]
* descr the pointer to the sparse CSC matrix descriptor.
* @param[in]
* rows number of rows in the CSC matrix.
* @param[in]
* cols number of columns in the CSC matrix
* @param[in]
* nnz number of non-zeros in the CSC matrix.
* @param[in]
* csc_col_ptr column offsets of the CSC matrix (must be array of length \p cols+1 ).
* @param[in]
* csc_row_ind row indices of the CSC matrix (must be array of length \p nnz ).
* @param[in]
* csc_val values of the CSC matrix (must be array of length \p nnz ).
* @param[in]
* col_ptr_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* row_ind_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p csc_col_ptr or \p csc_row_ind or \p csc_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p nnz is invalid.
* \retval rocsparse_status_invalid_value if \p col_ptr_type or \p row_ind_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_csc_descr(rocsparse_spmat_descr* descr,
int64_t rows,
int64_t cols,
int64_t nnz,
void* csc_col_ptr,
void* csc_row_ind,
void* csc_val,
rocsparse_indextype col_ptr_type,
rocsparse_indextype row_ind_type,
rocsparse_index_base idx_base,
rocsparse_datatype data_type);
/*! \ingroup aux_module
* \brief Create a sparse ELL matrix descriptor
* \details
* \p rocsparse_create_ell_descr creates a sparse ELL matrix descriptor. It should be
* destroyed at the end using \p rocsparse_destroy_spmat_descr.
*
* @param[out]
* descr the pointer to the sparse ELL matrix descriptor.
* @param[in]
* rows number of rows in the ELL matrix.
* @param[in]
* cols number of columns in the ELL matrix
* @param[in]
* ell_col_ind column indices of the ELL matrix (must be array of length \p rows*ell_width ).
* @param[in]
* ell_val values of the ELL matrix (must be array of length \p rows*ell_width ).
* @param[in]
* ell_width width of the ELL matrix.
* @param[in]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p ell_col_ind or \p ell_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p ell_width is invalid.
* \retval rocsparse_status_invalid_value if \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_ell_descr(rocsparse_spmat_descr* descr,
int64_t rows,
int64_t cols,
void* ell_col_ind,
void* ell_val,
int64_t ell_width,
rocsparse_indextype idx_type,
rocsparse_index_base idx_base,
rocsparse_datatype data_type);
/*! \ingroup aux_module
* \brief Create a sparse blocked ELL matrix descriptor
* \details
* \p rocsparse_create_bell_descr creates a sparse blocked ELL matrix descriptor. It should be
* destroyed at the end using \p rocsparse_destroy_spmat_descr.
*
* @param[out]
* descr the pointer to the sparse blocked ELL matrix descriptor.
* @param[in]
* rows number of rows in the blocked ELL matrix.
* @param[in]
* cols number of columns in the blocked ELL matrix
* @param[in]
* ell_block_dir \ref rocsparse_direction_row or \ref rocsparse_direction_column.
* @param[in]
* ell_block_dim block dimension of the sparse blocked ELL matrix.
* @param[in]
* ell_cols column indices of the blocked ELL matrix (must be array of length \p rows*ell_width ).
* @param[in]
* ell_col_ind column indices of the blocked ELL matrix (must be array of length \p rows*ell_width ).
* @param[in]
* ell_val values of the blocked ELL matrix (must be array of length \p rows*ell_width ).
* @param[in]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[in]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p ell_cols or \p ell_col_ind or \p ell_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols is invalid.
* \retval rocsparse_status_invalid_value if \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_bell_descr(rocsparse_spmat_descr* descr,
int64_t rows,
int64_t cols,
rocsparse_direction ell_block_dir,
int64_t ell_block_dim,
int64_t ell_cols,
void* ell_col_ind,
void* ell_val,
rocsparse_indextype idx_type,
rocsparse_index_base idx_base,
rocsparse_datatype data_type);
/*! \ingroup aux_module
* \brief Destroy a sparse matrix descriptor
*
* \details
* \p rocsparse_destroy_spmat_descr destroys a sparse matrix descriptor and releases all
* resources used by the descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_destroy_spmat_descr(rocsparse_spmat_descr descr);
/*! \ingroup aux_module
* \brief Get the fields of the sparse COO matrix descriptor
* \details
* \p rocsparse_coo_get gets the fields of the sparse COO matrix descriptor
*
* @param[in]
* descr the pointer to the sparse COO matrix descriptor.
* @param[out]
* rows number of rows in the sparse COO matrix.
* @param[out]
* cols number of columns in the sparse COO matrix.
* @param[out]
* nnz number of non-zeros in sparse COO matrix.
* @param[out]
* coo_row_ind row indices of the COO matrix (must be array of length \p nnz ).
* @param[out]
* coo_col_ind column indices of the COO matrix (must be array of length \p nnz ).
* @param[out]
* coo_val values of the COO matrix (must be array of length \p nnz ).
* @param[out]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[out]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[out]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p coo_row_ind or \p coo_col_ind or \p coo_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p nnz is invalid.
* \retval rocsparse_status_invalid_value if \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_coo_get(const rocsparse_spmat_descr descr,
int64_t* rows,
int64_t* cols,
int64_t* nnz,
void** coo_row_ind,
void** coo_col_ind,
void** coo_val,
rocsparse_indextype* idx_type,
rocsparse_index_base* idx_base,
rocsparse_datatype* data_type);
/*! \ingroup aux_module
* \brief Get the fields of the sparse COO AoS matrix descriptor
* \details
* \p rocsparse_coo_aos_get gets the fields of the sparse COO AoS matrix descriptor
*
* @param[in]
* descr the pointer to the sparse COO AoS matrix descriptor.
* @param[out]
* rows number of rows in the sparse COO AoS matrix.
* @param[out]
* cols number of columns in the sparse COO AoS matrix.
* @param[out]
* nnz number of non-zeros in sparse COO AoS matrix.
* @param[out]
* coo_ind <row, columns> indices of the COO AoS matrix (must be array of length \p nnz ).
* @param[out]
* coo_val values of the COO AoS matrix (must be array of length \p nnz ).
* @param[out]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[out]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[out]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p coo_ind or \p coo_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p nnz is invalid.
* \retval rocsparse_status_invalid_value if \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_coo_aos_get(const rocsparse_spmat_descr descr,
int64_t* rows,
int64_t* cols,
int64_t* nnz,
void** coo_ind,
void** coo_val,
rocsparse_indextype* idx_type,
rocsparse_index_base* idx_base,
rocsparse_datatype* data_type);
/*! \ingroup aux_module
* \brief Get the fields of the sparse CSR matrix descriptor
* \details
* \p rocsparse_csr_get gets the fields of the sparse CSR matrix descriptor
*
* @param[in]
* descr the pointer to the sparse CSR matrix descriptor.
* @param[out]
* rows number of rows in the CSR matrix.
* @param[out]
* cols number of columns in the CSR matrix
* @param[out]
* nnz number of non-zeros in the CSR matrix.
* @param[out]
* csr_row_ptr row offsets of the CSR matrix (must be array of length \p rows+1 ).
* @param[out]
* csr_col_ind column indices of the CSR matrix (must be array of length \p nnz ).
* @param[out]
* csr_val values of the CSR matrix (must be array of length \p nnz ).
* @param[out]
* row_ptr_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[out]
* col_ind_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[out]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[out]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p csr_row_ptr or \p csr_col_ind or \p csr_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p nnz is invalid.
* \retval rocsparse_status_invalid_value if \p row_ptr_type or \p col_ind_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_csr_get(const rocsparse_spmat_descr descr,
int64_t* rows,
int64_t* cols,
int64_t* nnz,
void** csr_row_ptr,
void** csr_col_ind,
void** csr_val,
rocsparse_indextype* row_ptr_type,
rocsparse_indextype* col_ind_type,
rocsparse_index_base* idx_base,
rocsparse_datatype* data_type);
/*! \ingroup aux_module
* \brief Get the fields of the sparse ELL matrix descriptor
* \details
* \p rocsparse_ell_get gets the fields of the sparse ELL matrix descriptor
*
* @param[in]
* descr the pointer to the sparse ELL matrix descriptor.
* @param[out]
* rows number of rows in the ELL matrix.
* @param[out]
* cols number of columns in the ELL matrix
* @param[out]
* ell_col_ind column indices of the ELL matrix (must be array of length \p rows*ell_width ).
* @param[out]
* ell_val values of the ELL matrix (must be array of length \p rows*ell_width ).
* @param[out]
* ell_width width of the ELL matrix.
* @param[out]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[out]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[out]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p ell_col_ind or \p ell_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p ell_width is invalid.
* \retval rocsparse_status_invalid_value if \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_ell_get(const rocsparse_spmat_descr descr,
int64_t* rows,
int64_t* cols,
void** ell_col_ind,
void** ell_val,
int64_t* ell_width,
rocsparse_indextype* idx_type,
rocsparse_index_base* idx_base,
rocsparse_datatype* data_type);
/*! \ingroup aux_module
* \brief Get the fields of the sparse blocked ELL matrix descriptor
* \details
* \p rocsparse_bell_get gets the fields of the sparse blocked ELL matrix descriptor
*
* @param[in]
* descr the pointer to the sparse blocked ELL matrix descriptor.
* @param[out]
* rows number of rows in the blocked ELL matrix.
* @param[out]
* cols number of columns in the blocked ELL matrix
* @param[out]
* ell_block_dir \ref rocsparse_direction_row or \ref rocsparse_direction_column.
* @param[out]
* ell_block_dim block dimension of the sparse blocked ELL matrix.
* @param[out]
* ell_cols column indices of the blocked ELL matrix (must be array of length \p rows*ell_width ).
* @param[out]
* ell_col_ind column indices of the blocked ELL matrix (must be array of length \p rows*ell_width ).
* @param[out]
* ell_val values of the blocked ELL matrix (must be array of length \p rows*ell_width ).
* @param[out]
* idx_type \ref rocsparse_indextype_i32 or \ref rocsparse_indextype_i64.
* @param[out]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one.
* @param[out]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p ell_cols or \p ell_col_ind or \p ell_val is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p ell_block_dim is invalid.
* \retval rocsparse_status_invalid_value if \p ell_block_dir or \p idx_type or \p idx_base or \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_bell_get(const rocsparse_spmat_descr descr,
int64_t* rows,
int64_t* cols,
rocsparse_direction* ell_block_dir,
int64_t* ell_block_dim,
int64_t* ell_cols,
void** ell_col_ind,
void** ell_val,
rocsparse_indextype* idx_type,
rocsparse_index_base* idx_base,
rocsparse_datatype* data_type);
/*! \ingroup aux_module
* \brief Set the row indices, column indices and values array in the sparse COO matrix descriptor
*
* @param[inout]
* descr the pointer to the sparse vector descriptor.
* @param[in]
* coo_row_ind row indices of the COO matrix (must be array of length \p nnz ).
* @param[in]
* coo_col_ind column indices of the COO matrix (must be array of length \p nnz ).
* @param[in]
* coo_val values of the COO matrix (must be array of length \p nnz ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p coo_row_ind or \p coo_col_ind or \p coo_val is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_coo_set_pointers(rocsparse_spmat_descr descr,
void* coo_row_ind,
void* coo_col_ind,
void* coo_val);
/*! \ingroup aux_module
* \brief Set the <row, column> indices and values array in the sparse COO AoS matrix descriptor
*
* @param[inout]
* descr the pointer to the sparse vector descriptor.
* @param[in]
* coo_ind <row, column> indices of the COO matrix (must be array of length \p nnz ).
* @param[in]
* coo_val values of the COO matrix (must be array of length \p nnz ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p coo_ind or \p coo_val is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status
rocsparse_coo_aos_set_pointers(rocsparse_spmat_descr descr, void* coo_ind, void* coo_val);
/*! \ingroup aux_module
* \brief Set the row offsets, column indices and values array in the sparse CSR matrix descriptor
*
* @param[inout]
* descr the pointer to the sparse vector descriptor.
* @param[in]
* csr_row_ptr row offsets of the CSR matrix (must be array of length \p rows+1 ).
* @param[in]
* csr_col_ind column indices of the CSR matrix (must be array of length \p nnz ).
* @param[in]
* csr_val values of the CSR matrix (must be array of length \p nnz ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p coo_ind or \p coo_val is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_csr_set_pointers(rocsparse_spmat_descr descr,
void* csr_row_ptr,
void* csr_col_ind,
void* csr_val);
/*! \ingroup aux_module
* \brief Set the column offsets, row indices and values array in the sparse CSC matrix descriptor
*
* @param[inout]
* descr the pointer to the sparse vector descriptor.
* @param[in]
* csc_col_ptr column offsets of the CSC matrix (must be array of length \p cols+1 ).
* @param[in]
* csc_row_ind row indices of the CSC matrix (must be array of length \p nnz ).
* @param[in]
* csc_val values of the CSC matrix (must be array of length \p nnz ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p csc_col_ptr or \p csc_row_ind or \p csc_val is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_csc_set_pointers(rocsparse_spmat_descr descr,
void* csc_col_ptr,
void* csc_row_ind,
void* csc_val);
/*! \ingroup aux_module
* \brief Set the column indices and values array in the sparse ELL matrix descriptor
*
* @param[inout]
* descr the pointer to the sparse vector descriptor.
* @param[in]
* ell_col_ind column indices of the ELL matrix (must be array of length \p rows*ell_width ).
* @param[in]
* ell_val values of the ELL matrix (must be array of length \p rows*ell_width ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p ell_col_ind or \p ell_val is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status
rocsparse_ell_set_pointers(rocsparse_spmat_descr descr, void* ell_col_ind, void* ell_val);
/*! \ingroup aux_module
* \brief Get the number of rows, columns and non-zeros from the sparse matrix descriptor
*
* @param[in]
* descr the pointer to the sparse matrix descriptor.
* @param[out]
* rows number of rows in the sparse matrix.
* @param[out]
* cols number of columns in the sparse matrix.
* @param[out]
* nnz number of non-zeros in sparse matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p nnz is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spmat_get_size(rocsparse_spmat_descr descr,
int64_t* rows,
int64_t* cols,
int64_t* nnz);
/*! \ingroup aux_module
* \brief Get the sparse matrix format from the sparse matrix descriptor
*
* @param[in]
* descr the pointer to the sparse matrix descriptor.
* @param[out]
* format \ref rocsparse_format_coo or \ref rocsparse_format_coo_aos or
* \ref rocsparse_format_csr or \ref rocsparse_format_csc or
* \ref rocsparse_format_ell
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_value if \p format is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spmat_get_format(const rocsparse_spmat_descr descr,
rocsparse_format* format);
/*! \ingroup aux_module
* \brief Get the sparse matrix index base from the sparse matrix descriptor
*
* @param[in]
* descr the pointer to the sparse matrix descriptor.
* @param[out]
* idx_base \ref rocsparse_index_base_zero or \ref rocsparse_index_base_one
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_value if \p idx_base is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spmat_get_index_base(const rocsparse_spmat_descr descr,
rocsparse_index_base* idx_base);
/*! \ingroup aux_module
* \brief Get the values array from the sparse matrix descriptor
*
* @param[in]
* descr the pointer to the sparse matrix descriptor.
* @param[out]
* values values array of the sparse matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p values is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spmat_get_values(rocsparse_spmat_descr descr, void** values);
/*! \ingroup aux_module
* \brief Set the values array in the sparse matrix descriptor
*
* @param[inout]
* descr the pointer to the sparse matrix descriptor.
* @param[in]
* values values array of the sparse matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p values is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spmat_set_values(rocsparse_spmat_descr descr, void* values);
/*! \ingroup aux_module
* \brief Get the strided batch count from the sparse matrix descriptor
*
* @param[in]
* descr the pointer to the sparse matrix descriptor.
* @param[out]
* batch_count batch_count of the sparse matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_size if \p batch_count is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spmat_get_strided_batch(rocsparse_spmat_descr descr, int* batch_count);
/*! \ingroup aux_module
* \brief Set the strided batch count in the sparse matrix descriptor
*
* @param[in]
* descr the pointer to the sparse matrix descriptor.
* @param[in]
* batch_count batch_count of the sparse matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_size if \p batch_count is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spmat_set_strided_batch(rocsparse_spmat_descr descr, int batch_count);
/*! \ingroup aux_module
* \brief Set the batch count and batch stride in the sparse COO matrix descriptor
*
* @param[inout]
* descr the pointer to the sparse COO matrix descriptor.
* @param[in]
* batch_count batch_count of the sparse COO matrix.
* @param[in]
* batch_stride batch stride of the sparse COO matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_size if \p batch_count or \p batch_stride is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_coo_set_strided_batch(rocsparse_spmat_descr descr,
int batch_count,
int64_t batch_stride);
/*! \ingroup aux_module
* \brief Set the batch count, row offset batch stride and the column indices batch stride in the sparse CSR matrix descriptor
*
* @param[inout]
* descr the pointer to the sparse CSR matrix descriptor.
* @param[in]
* batch_count batch_count of the sparse CSR matrix.
* @param[in]
* offsets_batch_stride row offset batch stride of the sparse CSR matrix.
* @param[in]
* offsets_batch_stride column indices batch stride of the sparse CSR matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_size if \p batch_count or \p offsets_batch_stride or \p columns_values_batch_stride is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_csr_set_strided_batch(rocsparse_spmat_descr descr,
int batch_count,
int64_t offsets_batch_stride,
int64_t columns_values_batch_stride);
/*! \ingroup aux_module
* \brief Get the requested attribute data from the sparse matrix descriptor
*
* @param[in]
* descr the pointer to the sparse matrix descriptor.
* @param[in]
* attribute \ref rocsparse_spmat_fill_mode or \ref rocsparse_spmat_diag_type or
* \ref rocsparse_spmat_matrix_type or \ref rocsparse_spmat_storage_mode
* @param[out]
* data attribute data
* @param[in]
* data_size attribute data size.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p data is invalid.
* \retval rocsparse_status_invalid_value if \p attribute is invalid.
* \retval rocsparse_status_invalid_size if \p data_size is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_csc_set_strided_batch(rocsparse_spmat_descr descr,
int batch_count,
int64_t offsets_batch_stride,
int64_t rows_values_batch_stride);
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spmat_get_attribute(rocsparse_spmat_descr descr,
rocsparse_spmat_attribute attribute,
void* data,
size_t data_size);
/*! \ingroup aux_module
* \brief Set the requested attribute data in the sparse matrix descriptor
*
* @param[inout]
* descr the pointer to the sparse matrix descriptor.
* @param[in]
* attribute \ref rocsparse_spmat_fill_mode or \ref rocsparse_spmat_diag_type or
* \ref rocsparse_spmat_matrix_type or \ref rocsparse_spmat_storage_mode
* @param[in]
* data attribute data
* @param[in]
* data_size attribute data size.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p data is invalid.
* \retval rocsparse_status_invalid_value if \p attribute is invalid.
* \retval rocsparse_status_invalid_size if \p data_size is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_spmat_set_attribute(rocsparse_spmat_descr descr,
rocsparse_spmat_attribute attribute,
const void* data,
size_t data_size);
/*! \ingroup aux_module
* \brief Create a dense vector descriptor
* \details
* \p rocsparse_create_dnvec_descr creates a dense vector descriptor. It should be
* destroyed at the end using rocsparse_create_dnvec_descr().
*
* @param[out]
* descr the pointer to the dense vector descriptor.
* @param[in]
* size size of the dense vector.
* @param[in]
* values non-zero values in the dense vector (must be array of length \p size ).
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p values is invalid.
* \retval rocsparse_status_invalid_size if \p size is invalid.
* \retval rocsparse_status_invalid_value if \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_dnvec_descr(rocsparse_dnvec_descr* descr,
int64_t size,
void* values,
rocsparse_datatype data_type);
/*! \ingroup aux_module
* \brief Destroy a dense vector descriptor
*
* \details
* \p rocsparse_destroy_dnvec_descr destroys a dense vector descriptor and releases all
* resources used by the descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_destroy_dnvec_descr(rocsparse_dnvec_descr descr);
/*! \ingroup aux_module
* \brief Get the fields of the dense vector descriptor
* \details
* \p rocsparse_dnvec_get gets the fields of the dense vector descriptor
*
* @param[in]
* descr the pointer to the dense vector descriptor.
* @param[out]
* size size of the dense vector.
* @param[out]
* values non-zero values in the dense vector (must be array of length \p size ).
* @param[out]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p values is invalid.
* \retval rocsparse_status_invalid_size if \p size is invalid.
* \retval rocsparse_status_invalid_value if \p data_type is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_dnvec_get(const rocsparse_dnvec_descr descr,
int64_t* size,
void** values,
rocsparse_datatype* data_type);
/*! \ingroup aux_module
* \brief Get the values array from a dense vector descriptor
*
* @param[in]
* descr the matrix descriptor.
* @param[out]
* values non-zero values in the dense vector (must be array of length \p size ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr or \p values is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_dnvec_get_values(const rocsparse_dnvec_descr descr, void** values);
/*! \ingroup aux_module
* \brief Set the values array in a dense vector descriptor
*
* @param[inout]
* descr the matrix descriptor.
* @param[in]
* values non-zero values in the dense vector (must be array of length \p size ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr or \p values is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_dnvec_set_values(rocsparse_dnvec_descr descr, void* values);
/*! \ingroup aux_module
* \brief Create a dense matrix descriptor
* \details
* \p rocsparse_create_dnmat_descr creates a dense matrix descriptor. It should be
* destroyed at the end using rocsparse_create_dnmat_descr().
*
* @param[out]
* descr the pointer to the dense matrix descriptor.
* @param[in]
* rows number of rows in the dense matrix.
* @param[in]
* cols number of columns in the dense matrix.
* @param[in]
* ld leading dimension of the dense matrix.
* @param[in]
* values non-zero values in the dense vector (must be array of length
* \p ld*rows if \p order=rocsparse_order_column or \p ld*cols if \p order=rocsparse_order_row ).
* @param[in]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
* @param[in]
* order \ref rocsparse_order_row or \ref rocsparse_order_column.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p values is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p ld is invalid.
* \retval rocsparse_status_invalid_value if \p data_type or \p order is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_create_dnmat_descr(rocsparse_dnmat_descr* descr,
int64_t rows,
int64_t cols,
int64_t ld,
void* values,
rocsparse_datatype data_type,
rocsparse_order order);
/*! \ingroup aux_module
* \brief Destroy a dense matrix descriptor
*
* \details
* \p rocsparse_destroy_dnmat_descr destroys a dense matrix descriptor and releases all
* resources used by the descriptor.
*
* @param[in]
* descr the matrix descriptor.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_destroy_dnmat_descr(rocsparse_dnmat_descr descr);
/*! \ingroup aux_module
* \brief Get the fields of the dense matrix descriptor
*
* @param[in]
* descr the pointer to the dense matrix descriptor.
* @param[out]
* rows number of rows in the dense matrix.
* @param[out]
* cols number of columns in the dense matrix.
* @param[out]
* ld leading dimension of the dense matrix.
* @param[out]
* values non-zero values in the dense matrix (must be array of length
* \p ld*rows if \p order=rocsparse_order_column or \p ld*cols if \p order=rocsparse_order_row ).
* @param[out]
* data_type \ref rocsparse_datatype_f32_r, \ref rocsparse_datatype_f64_r,
* \ref rocsparse_datatype_f32_c or \ref rocsparse_datatype_f64_c.
* @param[out]
* order \ref rocsparse_order_row or \ref rocsparse_order_column.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p values is invalid.
* \retval rocsparse_status_invalid_size if \p rows or \p cols or \p ld is invalid.
* \retval rocsparse_status_invalid_value if \p data_type or \p order is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_dnmat_get(const rocsparse_dnmat_descr descr,
int64_t* rows,
int64_t* cols,
int64_t* ld,
void** values,
rocsparse_datatype* data_type,
rocsparse_order* order);
/*! \ingroup aux_module
* \brief Get the values array from the dense matrix descriptor
*
* @param[in]
* descr the pointer to the dense matrix descriptor.
* @param[out]
* values non-zero values in the dense matrix (must be array of length
* \p ld*rows if \p order=rocsparse_order_column or \p ld*cols if \p order=rocsparse_order_row ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr or \p values is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_dnmat_get_values(const rocsparse_dnmat_descr descr, void** values);
/*! \ingroup aux_module
* \brief Set the values array in a dense matrix descriptor
*
* @param[inout]
* descr the matrix descriptor.
* @param[in]
* values non-zero values in the dense matrix (must be array of length
* \p ld*rows if \p order=rocsparse_order_column or \p ld*cols if \p order=rocsparse_order_row ).
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer \p descr or \p values is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_dnmat_set_values(rocsparse_dnmat_descr descr, void* values);
/*! \ingroup aux_module
* \brief Get the batch count and batch stride from the dense matrix descriptor
*
* @param[in]
* descr the pointer to the dense matrix descriptor.
* @param[out]
* batch_count the batch count in the dense matrix.
* @param[out]
* batch_stride the batch stride in the dense matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_size if \p batch_count or \p batch_stride is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_dnmat_get_strided_batch(rocsparse_dnmat_descr descr,
int* batch_count,
int64_t* batch_stride);
/*! \ingroup aux_module
* \brief Set the batch count and batch stride in the dense matrix descriptor
*
* @param[inout]
* descr the pointer to the dense matrix descriptor.
* @param[in]
* batch_count the batch count in the dense matrix.
* @param[in]
* batch_stride the batch stride in the dense matrix.
*
* \retval rocsparse_status_success the operation completed successfully.
* \retval rocsparse_status_invalid_pointer if \p descr is invalid.
* \retval rocsparse_status_invalid_size if \p batch_count or \p batch_stride is invalid.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_dnmat_set_strided_batch(rocsparse_dnmat_descr descr,
int batch_count,
int64_t batch_stride);
//
// If ROCSPARSE_WITH_MEMSTAT is defined
// then a set of extra routines is offered
// to manage memory with a recording of some traces.
//
#ifdef ROCSPARSE_WITH_MEMSTAT
/*! \ingroup aux_module
* \brief Set the memory report filename.
*
* \details
* \p rocsparse_memstat_report set the filename to use for the memory report.
* This routine is optional, but it must be called before any hip memory operation.
* Note that the default memory report filename is 'rocsparse_memstat.json'.
* Also note that if any operation occurs before calling this routine, the default filename rocsparse_memstat.json
* will be used but renamed after this call.
* The content of the memory report summarizes memory operations from the use of the routines
* \ref rocsparse_hip_malloc,
* \ref rocsparse_hip_free,
* \ref rocsparse_hip_host_malloc,
* \ref rocsparse_hip_host_free,
* \ref rocsparse_hip_host_managed,
* \ref rocsparse_hip_free_managed.
*
* @param[in]
* filename the memory report filename.
*
* \retval rocsparse_status_success the operation succeeded.
* \retval rocsparse_status_invalid_pointer \p handle filename is an invalid pointer.
* \retval rocsparse_status_internal_error an internal error occurred.
*/
ROCSPARSE_EXPORT
rocsparse_status rocsparse_memstat_report(const char* filename);
/*! \ingroup aux_module
* \brief Wrap hipFree.
*
* @param[in]
* mem memory pointer
* @param[in]
* tag tag to attach to the operation.
*
* \retval error from the related hip operation.
*/
ROCSPARSE_EXPORT
hipError_t rocsparse_hip_free(void* mem, const char* tag);
/*! \ingroup aux_module
* \brief Wrap hipMalloc.
*
* @param[in]
* mem pointer of memory pointer
* @param[in]
* nbytes number of bytes
* @param[in]
* tag tag to attach to the operation
*
* \retval error from the related hip operation
*/
ROCSPARSE_EXPORT
hipError_t rocsparse_hip_malloc(void** mem, size_t nbytes, const char* tag);
/*! \ingroup aux_module
* \brief Wrap hipHostFree.
*
* @param[in]
* mem memory pointer
* @param[in]
* tag tag to attach to the operation.
*
* \retval error from the related hip operation.
*/
ROCSPARSE_EXPORT
hipError_t rocsparse_hip_host_free(void* mem, const char* tag);
/*! \ingroup aux_module
* \brief Wrap hipHostMalloc.
*
* @param[in]
* mem pointer of memory pointer
* @param[in]
* nbytes number of bytes
* @param[in]
* tag tag to attach to the operation
*
* \retval error from the related hip operation
*/
ROCSPARSE_EXPORT
hipError_t rocsparse_hip_host_malloc(void** mem, size_t nbytes, const char* tag);
/*! \ingroup aux_module
* \brief Wrap hipFreeManaged.
*
* @param[in]
* mem memory pointer
* @param[in]
* tag tag to attach to the operation.
*
* \retval error from the related hip operation.
*/
ROCSPARSE_EXPORT
hipError_t rocsparse_hip_free_managed(void* mem, const char* tag);
/*! \ingroup aux_module
* \brief Wrap hipMallocManaged.
*
* @param[in]
* mem pointer of memory pointer
* @param[in]
* nbytes number of bytes
* @param[in]
* tag tag to attach to the operation
*
* \retval error from the related hip operation
*/
ROCSPARSE_EXPORT
hipError_t rocsparse_hip_malloc_managed(void** mem, size_t nbytes, const char* tag);
#endif
#ifdef __cplusplus
}
#endif
#endif /* _ROCSPARSE_AUXILIARY_H_ */
|