Skip to content

Commit

Permalink
Merge pull request #1124 from emankov/HIPIFY
Browse files Browse the repository at this point in the history
[HIPIFY][#675][#677][SOLVER][feature] cuSOLVER support - Step 4 - Data types
  • Loading branch information
emankov authored Nov 10, 2023
2 parents d8871bf + 9e01a6a commit 0132a6c
Show file tree
Hide file tree
Showing 9 changed files with 112 additions and 18 deletions.
34 changes: 28 additions & 6 deletions bin/hipify-perl
Original file line number Diff line number Diff line change
Expand Up @@ -1268,11 +1268,9 @@ sub experimentalSubstitutions {
subst("cusolverDnDgetrf", "hipsolverDnDgetrf", "library");
subst("cusolverDnDgetrf_bufferSize", "hipsolverDnDgetrf_bufferSize", "library");
subst("cusolverDnDgetrs", "hipsolverDnDgetrs", "library");
subst("cusolverDnHandle_t", "hipsolverHandle_t", "library");
subst("cusolverDnSgetrf", "hipsolverDnSgetrf", "library");
subst("cusolverDnSgetrf_bufferSize", "hipsolverDnSgetrf_bufferSize", "library");
subst("cusolverDnSgetrs", "hipsolverDnSgetrs", "library");
subst("cusolverStatus_t", "hipsolverStatus_t", "library");
subst("CUDA_EXT_SEM_SIGNAL_NODE_PARAMS", "hipExternalSemaphoreSignalNodeParams", "type");
subst("CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st", "hipExternalSemaphoreSignalNodeParams", "type");
subst("CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v1", "hipExternalSemaphoreSignalNodeParams", "type");
Expand All @@ -1287,6 +1285,18 @@ sub experimentalSubstitutions {
subst("cudaExternalSemaphoreSignalNodeParamsV2", "hipExternalSemaphoreSignalNodeParams", "type");
subst("cudaExternalSemaphoreWaitNodeParams", "hipExternalSemaphoreWaitNodeParams", "type");
subst("cudaExternalSemaphoreWaitNodeParamsV2", "hipExternalSemaphoreWaitNodeParams", "type");
subst("cusolverDnHandle_t", "hipsolverHandle_t", "type");
subst("cusolverStatus_t", "hipsolverStatus_t", "type");
subst("CUSOLVER_STATUS_ALLOC_FAILED", "HIPSOLVER_STATUS_ALLOC_FAILED", "numeric_literal");
subst("CUSOLVER_STATUS_ARCH_MISMATCH", "HIPSOLVER_STATUS_ARCH_MISMATCH", "numeric_literal");
subst("CUSOLVER_STATUS_EXECUTION_FAILED", "HIPSOLVER_STATUS_EXECUTION_FAILED", "numeric_literal");
subst("CUSOLVER_STATUS_INTERNAL_ERROR", "HIPSOLVER_STATUS_INTERNAL_ERROR", "numeric_literal");
subst("CUSOLVER_STATUS_INVALID_VALUE", "HIPSOLVER_STATUS_INVALID_VALUE", "numeric_literal");
subst("CUSOLVER_STATUS_MAPPING_ERROR", "HIPSOLVER_STATUS_MAPPING_ERROR", "numeric_literal");
subst("CUSOLVER_STATUS_NOT_INITIALIZED", "HIPSOLVER_STATUS_NOT_INITIALIZED", "numeric_literal");
subst("CUSOLVER_STATUS_NOT_SUPPORTED", "HIPSOLVER_STATUS_NOT_SUPPORTED", "numeric_literal");
subst("CUSOLVER_STATUS_SUCCESS", "HIPSOLVER_STATUS_SUCCESS", "numeric_literal");
subst("CUSOLVER_STATUS_ZERO_PIVOT", "HIPSOLVER_STATUS_ZERO_PIVOT", "numeric_literal");
subst("CU_DEVICE_ATTRIBUTE_HOST_REGISTER_SUPPORTED", "hipDeviceAttributeHostRegisterSupported", "numeric_literal");
subst("cudaDevAttrHostRegisterSupported", "hipDeviceAttributeHostRegisterSupported", "numeric_literal");
}
Expand Down Expand Up @@ -1761,8 +1771,6 @@ sub rocSubstitutions {
subst("cudnnTransformTensor", "miopenTransformTensor", "library");
subst("cusolverDnCreate", "rocblas_create_handle", "library");
subst("cusolverDnDestroy", "rocblas_destroy_handle", "library");
subst("cusolverDnHandle_t", "rocblas_handle", "library");
subst("cusolverStatus_t", "rocblas_status", "library");
subst("cusparseAxpby", "rocsparse_axpby", "library");
subst("cusparseBlockedEllGet", "rocsparse_bell_get", "library");
subst("cusparseCbsr2csr", "rocsparse_cbsr2csr", "library");
Expand Down Expand Up @@ -2145,6 +2153,8 @@ sub rocSubstitutions {
subst("cudnnSoftmaxMode_t", "miopenSoftmaxMode_t", "type");
subst("cudnnStatus_t", "miopenStatus_t", "type");
subst("cudnnTensorDescriptor_t", "miopenTensorDescriptor_t", "type");
subst("cusolverDnHandle_t", "rocblas_handle", "type");
subst("cusolverStatus_t", "rocblas_status", "type");
subst("cusparseAction_t", "rocsparse_action", "type");
subst("cusparseColorInfo", "_rocsparse_color_info", "type");
subst("cusparseColorInfo_t", "rocsparse_color_info", "type");
Expand Down Expand Up @@ -2206,10 +2216,10 @@ sub rocSubstitutions {
subst("CUBLAS_SIDE_LEFT", "rocblas_side_left", "numeric_literal");
subst("CUBLAS_SIDE_RIGHT", "rocblas_side_right", "numeric_literal");
subst("CUBLAS_STATUS_ALLOC_FAILED", "rocblas_status_not_implemented", "numeric_literal");
subst("CUBLAS_STATUS_ARCH_MISMATCH", "rocblas_status_size_query_mismatch", "numeric_literal");
subst("CUBLAS_STATUS_ARCH_MISMATCH", "rocblas_status_arch_mismatch", "numeric_literal");
subst("CUBLAS_STATUS_EXECUTION_FAILED", "rocblas_status_memory_error", "numeric_literal");
subst("CUBLAS_STATUS_INTERNAL_ERROR", "rocblas_status_internal_error", "numeric_literal");
subst("CUBLAS_STATUS_INVALID_VALUE", "rocblas_status_invalid_pointer", "numeric_literal");
subst("CUBLAS_STATUS_INVALID_VALUE", "rocblas_status_invalid_value", "numeric_literal");
subst("CUBLAS_STATUS_MAPPING_ERROR", "rocblas_status_invalid_size", "numeric_literal");
subst("CUBLAS_STATUS_NOT_INITIALIZED", "rocblas_status_invalid_handle", "numeric_literal");
subst("CUBLAS_STATUS_NOT_SUPPORTED", "rocblas_status_perf_degraded", "numeric_literal");
Expand Down Expand Up @@ -2302,6 +2312,16 @@ sub rocSubstitutions {
subst("CUDNN_STATUS_NOT_SUPPORTED", "miopenStatusUnsupportedOp", "numeric_literal");
subst("CUDNN_STATUS_SUCCESS", "miopenStatusSuccess", "numeric_literal");
subst("CUDNN_UNIDIRECTIONAL", "miopenRNNunidirection", "numeric_literal");
subst("CUSOLVER_STATUS_ALLOC_FAILED", "rocblas_status_memory_error", "numeric_literal");
subst("CUSOLVER_STATUS_ARCH_MISMATCH", "rocblas_status_arch_mismatch", "numeric_literal");
subst("CUSOLVER_STATUS_EXECUTION_FAILED", "rocblas_status_not_implemented", "numeric_literal");
subst("CUSOLVER_STATUS_INTERNAL_ERROR", "rocblas_status_internal_error", "numeric_literal");
subst("CUSOLVER_STATUS_INVALID_VALUE", "rocblas_status_invalid_value", "numeric_literal");
subst("CUSOLVER_STATUS_MAPPING_ERROR", "rocblas_status_not_implemented", "numeric_literal");
subst("CUSOLVER_STATUS_NOT_INITIALIZED", "rocblas_status_invalid_handle", "numeric_literal");
subst("CUSOLVER_STATUS_NOT_SUPPORTED", "rocblas_status_not_implemented", "numeric_literal");
subst("CUSOLVER_STATUS_SUCCESS", "rocblas_status_success", "numeric_literal");
subst("CUSOLVER_STATUS_ZERO_PIVOT", "rocblas_status_not_implemented", "numeric_literal");
subst("CUSPARSE_ACTION_NUMERIC", "rocsparse_action_numeric", "numeric_literal");
subst("CUSPARSE_ACTION_SYMBOLIC", "rocsparse_action_symbolic", "numeric_literal");
subst("CUSPARSE_DENSETOSPARSE_ALG_DEFAULT", "rocsparse_dense_to_sparse_alg_default", "numeric_literal");
Expand Down Expand Up @@ -8613,6 +8633,8 @@ sub warnUnsupportedFunctions {
"CUSPARSE_ALG_MERGE_PATH",
"CUSPARSE_ALG1",
"CUSPARSE_ALG0",
"CUSOLVER_STATUS_MATRIX_TYPE_NOT_SUPPORTED",
"CUSOLVER_STATUS_INVALID_LICENSE",
"CURAND_REJECTION",
"CURAND_POISSON",
"CURAND_ORDERING_QUASI_DEFAULT",
Expand Down
4 changes: 2 additions & 2 deletions docs/tables/CUBLAS_API_supported_by_HIP_and_ROC.md
Original file line number Diff line number Diff line change
Expand Up @@ -79,10 +79,10 @@
|`CUBLAS_SIDE_LEFT`| | | | |`HIPBLAS_SIDE_LEFT`|1.8.2| | | | |`rocblas_side_left`|1.5.0| | | | |
|`CUBLAS_SIDE_RIGHT`| | | | |`HIPBLAS_SIDE_RIGHT`|1.8.2| | | | |`rocblas_side_right`|1.5.0| | | | |
|`CUBLAS_STATUS_ALLOC_FAILED`| | | | |`HIPBLAS_STATUS_ALLOC_FAILED`|1.8.2| | | | |`rocblas_status_not_implemented`|1.5.0| | | | |
|`CUBLAS_STATUS_ARCH_MISMATCH`| | | | |`HIPBLAS_STATUS_ARCH_MISMATCH`|1.8.2| | | | |`rocblas_status_size_query_mismatch`|3.5.0| | | | |
|`CUBLAS_STATUS_ARCH_MISMATCH`| | | | |`HIPBLAS_STATUS_ARCH_MISMATCH`|1.8.2| | | | |`rocblas_status_arch_mismatch`|5.7.0| | | | |
|`CUBLAS_STATUS_EXECUTION_FAILED`| | | | |`HIPBLAS_STATUS_EXECUTION_FAILED`|1.8.2| | | | |`rocblas_status_memory_error`|1.5.0| | | | |
|`CUBLAS_STATUS_INTERNAL_ERROR`| | | | |`HIPBLAS_STATUS_INTERNAL_ERROR`|1.8.2| | | | |`rocblas_status_internal_error`|1.5.0| | | | |
|`CUBLAS_STATUS_INVALID_VALUE`| | | | |`HIPBLAS_STATUS_INVALID_VALUE`|1.8.2| | | | |`rocblas_status_invalid_pointer`|1.5.0| | | | |
|`CUBLAS_STATUS_INVALID_VALUE`| | | | |`HIPBLAS_STATUS_INVALID_VALUE`|1.8.2| | | | |`rocblas_status_invalid_value`|3.5.0| | | | |
|`CUBLAS_STATUS_LICENSE_ERROR`| | | | |`HIPBLAS_STATUS_UNKNOWN`| | | | | | | | | | | |
|`CUBLAS_STATUS_MAPPING_ERROR`| | | | |`HIPBLAS_STATUS_MAPPING_ERROR`|1.8.2| | | | |`rocblas_status_invalid_size`|1.5.0| | | | |
|`CUBLAS_STATUS_NOT_INITIALIZED`| | | | |`HIPBLAS_STATUS_NOT_INITIALIZED`|1.8.2| | | | |`rocblas_status_invalid_handle`|1.5.0| | | | |
Expand Down
4 changes: 2 additions & 2 deletions docs/tables/CUBLAS_API_supported_by_ROC.md
Original file line number Diff line number Diff line change
Expand Up @@ -79,10 +79,10 @@
|`CUBLAS_SIDE_LEFT`| | | | |`rocblas_side_left`|1.5.0| | | | |
|`CUBLAS_SIDE_RIGHT`| | | | |`rocblas_side_right`|1.5.0| | | | |
|`CUBLAS_STATUS_ALLOC_FAILED`| | | | |`rocblas_status_not_implemented`|1.5.0| | | | |
|`CUBLAS_STATUS_ARCH_MISMATCH`| | | | |`rocblas_status_size_query_mismatch`|3.5.0| | | | |
|`CUBLAS_STATUS_ARCH_MISMATCH`| | | | |`rocblas_status_arch_mismatch`|5.7.0| | | | |
|`CUBLAS_STATUS_EXECUTION_FAILED`| | | | |`rocblas_status_memory_error`|1.5.0| | | | |
|`CUBLAS_STATUS_INTERNAL_ERROR`| | | | |`rocblas_status_internal_error`|1.5.0| | | | |
|`CUBLAS_STATUS_INVALID_VALUE`| | | | |`rocblas_status_invalid_pointer`|1.5.0| | | | |
|`CUBLAS_STATUS_INVALID_VALUE`| | | | |`rocblas_status_invalid_value`|3.5.0| | | | |
|`CUBLAS_STATUS_LICENSE_ERROR`| | | | | | | | | | |
|`CUBLAS_STATUS_MAPPING_ERROR`| | | | |`rocblas_status_invalid_size`|1.5.0| | | | |
|`CUBLAS_STATUS_NOT_INITIALIZED`| | | | |`rocblas_status_invalid_handle`|1.5.0| | | | |
Expand Down
6 changes: 4 additions & 2 deletions src/CUDA2HIP_BLAS_API_types.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -38,12 +38,12 @@ const std::map<llvm::StringRef, hipCounter> CUDA_BLAS_TYPE_NAME_MAP {
{"CUBLAS_STATUS_SUCCESS", {"HIPBLAS_STATUS_SUCCESS", "rocblas_status_success", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_NOT_INITIALIZED", {"HIPBLAS_STATUS_NOT_INITIALIZED", "rocblas_status_invalid_handle", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_ALLOC_FAILED", {"HIPBLAS_STATUS_ALLOC_FAILED", "rocblas_status_not_implemented", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_INVALID_VALUE", {"HIPBLAS_STATUS_INVALID_VALUE", "rocblas_status_invalid_pointer", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_INVALID_VALUE", {"HIPBLAS_STATUS_INVALID_VALUE", "rocblas_status_invalid_value", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_MAPPING_ERROR", {"HIPBLAS_STATUS_MAPPING_ERROR", "rocblas_status_invalid_size", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_EXECUTION_FAILED", {"HIPBLAS_STATUS_EXECUTION_FAILED", "rocblas_status_memory_error", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_INTERNAL_ERROR", {"HIPBLAS_STATUS_INTERNAL_ERROR", "rocblas_status_internal_error", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_NOT_SUPPORTED", {"HIPBLAS_STATUS_NOT_SUPPORTED", "rocblas_status_perf_degraded", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_ARCH_MISMATCH", {"HIPBLAS_STATUS_ARCH_MISMATCH", "rocblas_status_size_query_mismatch", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_ARCH_MISMATCH", {"HIPBLAS_STATUS_ARCH_MISMATCH", "rocblas_status_arch_mismatch", CONV_NUMERIC_LITERAL, API_BLAS, 2}},
{"CUBLAS_STATUS_LICENSE_ERROR", {"HIPBLAS_STATUS_UNKNOWN", "rocblas_status_not_implemented", CONV_NUMERIC_LITERAL, API_BLAS, 2, ROC_UNSUPPORTED}},

// Blas Fill Modes
Expand Down Expand Up @@ -389,6 +389,8 @@ const std::map<llvm::StringRef, hipAPIversions> HIP_BLAS_TYPE_NAME_VER_MAP {
{"rocblas_status_internal_error", {HIP_1050, HIP_0, HIP_0 }},
{"rocblas_status_perf_degraded", {HIP_3050, HIP_0, HIP_0 }},
{"rocblas_status_size_query_mismatch", {HIP_3050, HIP_0, HIP_0 }},
{"rocblas_status_arch_mismatch", {HIP_5070, HIP_0, HIP_0 }},
{"rocblas_status_invalid_value", {HIP_3050, HIP_0, HIP_0 }},
{"rocblas_datatype", {HIP_1082, HIP_0, HIP_0 }},
{"rocblas_datatype_", {HIP_1082, HIP_0, HIP_0 }},
{"rocblas_datatype_f16_r", {HIP_1082, HIP_0, HIP_0 }},
Expand Down
34 changes: 32 additions & 2 deletions src/CUDA2HIP_SOLVER_API_types.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -24,14 +24,44 @@ THE SOFTWARE.

// Map of all functions
const std::map<llvm::StringRef, hipCounter> CUDA_SOLVER_TYPE_NAME_MAP {
{"cusolverStatus_t", {"hipsolverStatus_t", "rocblas_status", CONV_LIB_FUNC, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"cusolverDnHandle_t", {"hipsolverHandle_t", "rocblas_handle", CONV_LIB_FUNC, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"cusolverStatus_t", {"hipsolverStatus_t", "rocblas_status", CONV_TYPE, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_SUCCESS", {"HIPSOLVER_STATUS_SUCCESS", "rocblas_status_success", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_NOT_INITIALIZED", {"HIPSOLVER_STATUS_NOT_INITIALIZED", "rocblas_status_invalid_handle", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_ALLOC_FAILED", {"HIPSOLVER_STATUS_ALLOC_FAILED", "rocblas_status_memory_error", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_INVALID_VALUE", {"HIPSOLVER_STATUS_INVALID_VALUE", "rocblas_status_invalid_value", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_ARCH_MISMATCH", {"HIPSOLVER_STATUS_ARCH_MISMATCH", "rocblas_status_arch_mismatch", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_MAPPING_ERROR", {"HIPSOLVER_STATUS_MAPPING_ERROR", "rocblas_status_not_implemented", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_EXECUTION_FAILED", {"HIPSOLVER_STATUS_EXECUTION_FAILED", "rocblas_status_not_implemented", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_INTERNAL_ERROR", {"HIPSOLVER_STATUS_INTERNAL_ERROR", "rocblas_status_internal_error", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_MATRIX_TYPE_NOT_SUPPORTED", {"HIPSOLVER_STATUS_MATRIX_TYPE_NOT_SUPPORTED", "rocblas_status_not_implemented", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}},
{"CUSOLVER_STATUS_NOT_SUPPORTED", {"HIPSOLVER_STATUS_NOT_SUPPORTED", "rocblas_status_not_implemented", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_ZERO_PIVOT", {"HIPSOLVER_STATUS_ZERO_PIVOT", "rocblas_status_not_implemented", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}},
{"CUSOLVER_STATUS_INVALID_LICENSE", {"HIPSOLVER_STATUS_INVALID_LICENSE", "rocblas_status_not_implemented", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}},
{"cusolverDnHandle_t", {"hipsolverHandle_t", "rocblas_handle", CONV_TYPE, API_SOLVER, 1, HIP_EXPERIMENTAL}},
};

const std::map<llvm::StringRef, cudaAPIversions> CUDA_SOLVER_TYPE_NAME_VER_MAP {
};

const std::map<llvm::StringRef, hipAPIversions> HIP_SOLVER_TYPE_NAME_VER_MAP {
{"hipsolverStatus_t", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"HIPSOLVER_STATUS_SUCCESS", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"HIPSOLVER_STATUS_NOT_INITIALIZED", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"HIPSOLVER_STATUS_ALLOC_FAILED", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"HIPSOLVER_STATUS_INVALID_VALUE", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"HIPSOLVER_STATUS_ARCH_MISMATCH", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"HIPSOLVER_STATUS_MAPPING_ERROR", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"HIPSOLVER_STATUS_EXECUTION_FAILED", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"HIPSOLVER_STATUS_INTERNAL_ERROR", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"HIPSOLVER_STATUS_NOT_SUPPORTED", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"hipsolverHandle_t", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}},
{"rocblas_status", {HIP_3000, HIP_0, HIP_0, HIP_LATEST}},
{"rocblas_status_success", {HIP_3000, HIP_0, HIP_0, HIP_LATEST}},
{"rocblas_status_invalid_handle", {HIP_5060, HIP_0, HIP_0, HIP_LATEST}},
{"rocblas_status_memory_error", {HIP_5060, HIP_0, HIP_0, HIP_LATEST}},
{"rocblas_status_invalid_value", {HIP_3050, HIP_0, HIP_0, HIP_LATEST}},
{"rocblas_status_not_implemented", {HIP_1050, HIP_0, HIP_0, HIP_LATEST}},
{"rocblas_status_internal_error", {HIP_1050, HIP_0, HIP_0, HIP_LATEST}},
{"rocblas_status_arch_mismatch", {HIP_5070, HIP_0, HIP_0, HIP_LATEST}},
{"rocblas_handle", {HIP_1050, HIP_0, HIP_0, HIP_LATEST}},
};
4 changes: 2 additions & 2 deletions tests/unit_tests/synthetic/libraries/cublas2rocblas.cu
Original file line number Diff line number Diff line change
Expand Up @@ -24,12 +24,12 @@ int main() {
// CHECK-NEXT: rocblas_status BLAS_STATUS_SUCCESS = rocblas_status_success;
// CHECK-NEXT: rocblas_status BLAS_STATUS_NOT_INITIALIZED = rocblas_status_invalid_handle;
// CHECK-NEXT: rocblas_status BLAS_STATUS_ALLOC_FAILED = rocblas_status_not_implemented;
// CHECK-NEXT: rocblas_status BLAS_STATUS_INVALID_VALUE = rocblas_status_invalid_pointer;
// CHECK-NEXT: rocblas_status BLAS_STATUS_INVALID_VALUE = rocblas_status_invalid_value;
// CHECK-NEXT: rocblas_status BLAS_STATUS_MAPPING_ERROR = rocblas_status_invalid_size;
// CHECK-NEXT: rocblas_status BLAS_STATUS_EXECUTION_FAILED = rocblas_status_memory_error;
// CHECK-NEXT: rocblas_status BLAS_STATUS_INTERNAL_ERROR = rocblas_status_internal_error;
// CHECK-NEXT: rocblas_status BLAS_STATUS_NOT_SUPPORTED = rocblas_status_perf_degraded;
// CHECK-NEXT: rocblas_status BLAS_STATUS_ARCH_MISMATCH = rocblas_status_size_query_mismatch;
// CHECK-NEXT: rocblas_status BLAS_STATUS_ARCH_MISMATCH = rocblas_status_arch_mismatch;
cublasStatus blasStatus;
cublasStatus_t blasStatus_t;
cublasStatus_t BLAS_STATUS_SUCCESS = CUBLAS_STATUS_SUCCESS;
Expand Down
Loading

0 comments on commit 0132a6c

Please sign in to comment.