forked from ROCm/HIPIFY
-
Notifications
You must be signed in to change notification settings - Fork 0
Commit
This commit does not belong to any branch on this repository, and may belong to a fork outside of the repository.
[HIPIFY][ROCm#674][rocSPARSE][feature] rocSPARSE support - Step 103 -…
… `cusparseSpSM_analysis` -> `rocsparse_spsm` + [IMP] `rocsparse_spsm` has been changed in 6.0.0, so reflected that in HIPIFY, docs, and tests + Updated `SPARSE` synthetic tests, the regenerated hipify-perl, and `SPARSE` `CUDA2HIP` documentation
- Loading branch information
Showing
9 changed files
with
153 additions
and
5 deletions.
There are no files selected for viewing
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
114 changes: 114 additions & 0 deletions
114
tests/unit_tests/synthetic/libraries/cusparse2rocsparse_11030_12000.cu
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
| Original file line number | Diff line number | Diff line change |
|---|---|---|
| @@ -0,0 +1,114 @@ | ||
| // RUN: %run_test hipify "%s" "%t" %hipify_args 4 --skip-excluded-preprocessor-conditional-blocks --experimental --roc --use-hip-data-types %clang_args -ferror-limit=500 | ||
|
|
||
| // CHECK: #include <hip/hip_runtime.h> | ||
| #include <cuda_runtime.h> | ||
| // CHECK: #include "hip/hip_complex.h" | ||
| #include "cuComplex.h" | ||
| #include <stdio.h> | ||
| // CHECK: #include "rocsparse.h" | ||
| #include "cusparse.h" | ||
| // CHECK-NOT: #include "rocsparse.h" | ||
|
|
||
| int main() { | ||
| printf("18.1. cuSPARSE API to rocSPARSE API synthetic test\n"); | ||
|
|
||
| // CHECK: rocsparse_status status_t; | ||
| cusparseStatus_t status_t; | ||
|
|
||
| // CHECK: _rocsparse_handle *handle = nullptr; | ||
| // CHECK-NEXT: rocsparse_handle handle_t; | ||
| cusparseContext *handle = nullptr; | ||
| cusparseHandle_t handle_t; | ||
|
|
||
| // CHECK: _rocsparse_mat_descr *matDescr = nullptr; | ||
| // CHECK-NEXT: rocsparse_mat_descr matDescr_t, matDescr_t_2, matDescr_A, matDescr_B, matDescr_C, matDescr_D; | ||
| cusparseMatDescr *matDescr = nullptr; | ||
| cusparseMatDescr_t matDescr_t, matDescr_t_2, matDescr_A, matDescr_B, matDescr_C, matDescr_D; | ||
|
|
||
| // CHECK: rocsparse_operation opA, opB, opX; | ||
| cusparseOperation_t opA, opB, opX; | ||
|
|
||
| // CHECK: rocsparse_solve_policy solvePolicy_t; | ||
| cusparseSolvePolicy_t solvePolicy_t; | ||
|
|
||
| int m = 0; | ||
| int n = 0; | ||
| int k = 0; | ||
| int innz = 0; | ||
| int nnza = 0; | ||
| int nnzb = 0; | ||
| int nnzc = 0; | ||
| int nnzd = 0; | ||
| int csrRowPtrA = 0; | ||
| int csrRowPtrB = 0; | ||
| int csrRowPtrC = 0; | ||
| int csrRowPtrD = 0; | ||
| int csrColIndA = 0; | ||
| int csrColIndB = 0; | ||
| int csrColIndC = 0; | ||
| int csrColIndD = 0; | ||
| int bufferSizeInBytes = 0; | ||
| size_t bufferSize = 0; | ||
| double dA = 0.f; | ||
| double dB = 0.f; | ||
| double dAlpha = 0.f; | ||
| double dF = 0.f; | ||
| double dX = 0.f; | ||
| double dcsrSortedValA = 0.f; | ||
| double dcsrSortedValB = 0.f; | ||
| double dcsrSortedValC = 0.f; | ||
| double dcsrSortedValD = 0.f; | ||
| float fAlpha = 0.f; | ||
| float fA = 0.f; | ||
| float fB = 0.f; | ||
| float fF = 0.f; | ||
| float fX = 0.f; | ||
| float csrSortedValA = 0.f; | ||
| float csrSortedValB = 0.f; | ||
| float csrSortedValC = 0.f; | ||
| float csrSortedValD = 0.f; | ||
| void *alpha = nullptr; | ||
| void *pBuffer = nullptr; | ||
| void *tempBuffer = nullptr; | ||
|
|
||
| // TODO: should be rocsparse_double_complex | ||
| // TODO: add to TypeOverloads cuDoubleComplex -> rocsparse_double_complex under a new option --sparse | ||
| // CHECK: rocblas_double_complex dcomplex, dcomplexA, dcomplexAlpha, dcomplexB, dcomplexBeta, dcomplexC, dcomplexF, dcomplexX, dcomplexY, dComplexbsrSortedValA, dComplexbsrSortedValC, dComplexcsrSortedValA, dComplexcsrSortedValB, dComplexcsrSortedValC, dComplexcsrSortedValD, dcomplextol, dComplexbsrSortedVal, dComplexbscVal, dComplexcscSortedVal, dcomplexds, dcomplexdl, dcomplexd, dcomplexdu, dcomplexdw, dcomplexx, dcomplex_boost_val; | ||
| cuDoubleComplex dcomplex, dcomplexA, dcomplexAlpha, dcomplexB, dcomplexBeta, dcomplexC, dcomplexF, dcomplexX, dcomplexY, dComplexbsrSortedValA, dComplexbsrSortedValC, dComplexcsrSortedValA, dComplexcsrSortedValB, dComplexcsrSortedValC, dComplexcsrSortedValD, dcomplextol, dComplexbsrSortedVal, dComplexbscVal, dComplexcscSortedVal, dcomplexds, dcomplexdl, dcomplexd, dcomplexdu, dcomplexdw, dcomplexx, dcomplex_boost_val; | ||
|
|
||
| // TODO: should be rocsparse_double_complex | ||
| // TODO: add to TypeOverloads cuComplex -> rocsparse_float_complex under a new option --sparse | ||
| // CHECK: rocblas_float_complex complex, complexA, complexAlpha, complexB, complexBeta, complexC, complexF, complexX, complexY, complexbsrValA, complexbsrSortedValC, complexcsrSortedValA, complexcsrSortedValB, complexcsrSortedValC, complexcsrSortedValD, complextol, complexbsrSortedVal, complexbscVal, complexcscSortedVal, complexds, complexdl, complexd, complexdu, complexdw, complexx, complex_boost_val; | ||
| cuComplex complex, complexA, complexAlpha, complexB, complexBeta, complexC, complexF, complexX, complexY, complexbsrValA, complexbsrSortedValC, complexcsrSortedValA, complexcsrSortedValB, complexcsrSortedValC, complexcsrSortedValD, complextol, complexbsrSortedVal, complexbscVal, complexcscSortedVal, complexds, complexdl, complexd, complexdu, complexdw, complexx, complex_boost_val; | ||
|
|
||
| #if CUDA_VERSION >= 8000 | ||
| // TODO: [#899] There should be rocsparse_datatype instead of hipDataType | ||
| cudaDataType_t dataType_t; | ||
| cudaDataType dataType; | ||
| #endif | ||
|
|
||
| #if (CUDA_VERSION >= 10010 && CUDA_VERSION < 11000 && !defined(_WIN32)) || CUDA_VERSION >= 11000 | ||
| // CHECK: rocsparse_spmat_descr spMatDescr_t, spmatA, spmatB, spmatC; | ||
| cusparseSpMatDescr_t spMatDescr_t, spmatA, spmatB, spmatC; | ||
|
|
||
| // CHECK: rocsparse_dnmat_descr dnMatDescr_t, dnmatA, dnmatB, dnmatC; | ||
| cusparseDnMatDescr_t dnMatDescr_t, dnmatA, dnmatB, dnmatC; | ||
| #endif | ||
|
|
||
| #if CUDA_VERSION >= 11030 && CUSPARSE_VERSION >= 11600 | ||
| // CHECK: rocsparse_spsm_alg spSMAlg_t; | ||
| cusparseSpSMAlg_t spSMAlg_t; | ||
|
|
||
| // NOTE:cusparseSpSMDescr_t doesn't have a correspondence in rocSPARSE, the corresponding function argument is removed in the hipified call of the rocsparse_spsm function | ||
| cusparseSpSMDescr_t spSMDescr; | ||
|
|
||
| #if CUDA_VERSION < 12000 | ||
| // CUDA: cusparseStatus_t CUSPARSEAPI cusparseSpSM_analysis(cusparseHandle_t handle, cusparseOperation_t opA, cusparseOperation_t opB, const void* alpha, cusparseSpMatDescr_t matA, cusparseDnMatDescr_t matB, cusparseDnMatDescr_t matC, cudaDataType computeType, cusparseSpSMAlg_t alg, cusparseSpSMDescr_t spsmDescr, void* externalBuffer); | ||
| // ROC: ROCSPARSE_EXPORT rocsparse_status rocsparse_spsm(rocsparse_handle handle, rocsparse_operation trans_A, rocsparse_operation trans_B, const void* alpha, const rocsparse_spmat_descr matA, const rocsparse_dnmat_descr matB, const rocsparse_dnmat_descr matC, rocsparse_datatype compute_type, rocsparse_spsm_alg alg, rocsparse_spsm_stage stage, size_t* buffer_size, void* temp_buffer); | ||
| // CHECK: status_t = rocsparse_spsm(handle_t, opA, opB, alpha, spmatA, dnmatB, dnmatC, dataType, spSMAlg_t, rocsparse_spsm_stage_compute, nullptr, tempBuffer); | ||
| status_t = cusparseSpSM_analysis(handle_t, opA, opB, alpha, spmatA, dnmatB, dnmatC, dataType, spSMAlg_t, spSMDescr, tempBuffer); | ||
| #endif | ||
| #endif | ||
|
|
||
| return 0; | ||
| } |
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters