Skip to content

Commit

Permalink
Rename CULiP_cublas_profiling_control_array
Browse files Browse the repository at this point in the history
  • Loading branch information
@enp1s0
enp1s0 committed Sep 25, 2023
1 parent 8527da1 commit e8fe4fa
Show file tree
Hide file tree
Showing 18 changed files with 33 additions and 33 deletions.
24 changes: 12 additions & 12 deletions src/cublas.cu
View file
Original file line number Diff line number Diff line change
Expand Up @@ -92,23 +92,23 @@ void* CULiP_cublas_lib_handle_cache = NULL;
// Control profiling
// 0 = Profiling
// Otherwise = Not profiling
int CULiP_profiling_control_array[CULiP_cublas_enum_length] = {0};
int CULiP_cublas_profiling_control_array[CULiP_cublas_enum_length] = {0};

// Controler setter
void CULiP_enable_cublas_profiling(const CULiP_cublas_control_t target_function) {
CULiP_profiling_control_array[target_function] = 0;
CULiP_cublas_profiling_control_array[target_function] = 0;
}
void CULiP_disable_cublas_profiling(const CULiP_cublas_control_t target_function) {
CULiP_profiling_control_array[target_function] = 1;
CULiP_cublas_profiling_control_array[target_function] = 1;
}
void CULiP_enable_cublas_all_profiling() {
for (unsigned target_function = 0; target_function < CULiP_cublas_enum_length; target_function++) {
CULiP_profiling_control_array[target_function] = 0;
CULiP_cublas_profiling_control_array[target_function] = 0;
}
}
void CULiP_disable_cublas_all_profiling() {
for (unsigned target_function = 0; target_function < CULiP_cublas_enum_length; target_function++) {
CULiP_profiling_control_array[target_function] = 1;
CULiP_cublas_profiling_control_array[target_function] = 1;
}
}

Expand Down Expand Up @@ -258,7 +258,7 @@ cublasStatus_t cublasGemmEx(cublasHandle_t handle, cublasOperation_t transa,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int cutoff_flag = (CULiP_profiling_control_array[CULiP_cublasGemmEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUTOFF_THRESHOLD_ENV_NAME, false);
const int cutoff_flag = (CULiP_cublas_profiling_control_array[CULiP_cublasGemmEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUTOFF_THRESHOLD_ENV_NAME, false);
if (cutoff_flag) {
double threshold;
try {
Expand All @@ -274,7 +274,7 @@ cublasStatus_t cublasGemmEx(cublasHandle_t handle, cublasOperation_t transa,
}
}

const int profiling_flag = (CULiP_profiling_control_array[CULiP_cublasGemmEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULiP_cublasGemmEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasOperation_t, cublasOperation_t, int, int, int, const void*, const void*, cudaDataType_t, int, const void*, cudaDataType_t, int, const void*, void*, cudaDataType_t, int, cublasComputeType_t, cublasGemmAlgo_t);
Expand Down Expand Up @@ -311,7 +311,7 @@ cublasStatus_t cublasGemmEx(cublasHandle_t handle, cublasOperation_t transa,
CULiP_launch_function(cuda_stream, &CULiP_print_profile_result, (void*)&profile_result);
}

const int exp_stats_flag = (CULiP_profiling_control_array[CULiP_cublasGemmEx] == 0) && CULiP_is_profiling_enabled(CULIP_EXP_STATS_ENABLE_ENV_NAME, false);
const int exp_stats_flag = (CULiP_cublas_profiling_control_array[CULiP_cublasGemmEx] == 0) && CULiP_is_profiling_enabled(CULIP_EXP_STATS_ENABLE_ENV_NAME, false);
if (exp_stats_flag) {
cudaStream_t cuda_stream;
cublasGetStream(handle, &cuda_stream);
Expand Down Expand Up @@ -403,7 +403,7 @@ cublasStatus_t cublasGemmBatchedEx(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULiP_cublasGemmBatchedEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULiP_cublasGemmBatchedEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasOperation_t, cublasOperation_t, int, int, int, const void*, const void* const[], cudaDataType_t, int, const void* const[], cudaDataType_t, int, const void*, void* const[], cudaDataType_t, int, int, cublasComputeType_t, cublasGemmAlgo_t);
Expand Down Expand Up @@ -519,7 +519,7 @@ cublasStatus_t cublasGemmStridedBatchedEx(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int cutoff_flag = (CULiP_profiling_control_array[CULiP_cublasGemmStridedBatchedEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUTOFF_THRESHOLD_ENV_NAME, false);
const int cutoff_flag = (CULiP_cublas_profiling_control_array[CULiP_cublasGemmStridedBatchedEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUTOFF_THRESHOLD_ENV_NAME, false);
if (cutoff_flag) {
double threshold;
try {
Expand All @@ -537,7 +537,7 @@ cublasStatus_t cublasGemmStridedBatchedEx(cublasHandle_t handle,
}
}

const int profiling_flag = (CULiP_profiling_control_array[CULiP_cublasGemmStridedBatchedEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULiP_cublasGemmStridedBatchedEx] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasOperation_t, cublasOperation_t, int, int, int, const void*, const void*, cudaDataType_t, int, long long int, const void*, cudaDataType_t, int, long long int, const void*, void*, cudaDataType_t, int, long long int, int, cublasComputeType_t, cublasGemmAlgo_t);
Expand Down Expand Up @@ -574,7 +574,7 @@ cublasStatus_t cublasGemmStridedBatchedEx(cublasHandle_t handle,
CULiP_launch_function(cuda_stream, &CULiP_print_profile_result, (void*)&profile_result);
}

const int exp_stats_flag = (CULiP_profiling_control_array[CULiP_cublasGemmStridedBatchedEx] == 0) && CULiP_is_profiling_enabled(CULIP_EXP_STATS_ENABLE_ENV_NAME, false);
const int exp_stats_flag = (CULiP_cublas_profiling_control_array[CULiP_cublasGemmStridedBatchedEx] == 0) && CULiP_is_profiling_enabled(CULIP_EXP_STATS_ENABLE_ENV_NAME, false);
if (exp_stats_flag) {
cudaStream_t cuda_stream;
cublasGetStream(handle, &cuda_stream);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.gbmv.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -6,7 +6,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasOperation_t, int, int, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, const CULIP_TYPE*, CULIP_TYPE*, int);
Expand Down
6 changes: 3 additions & 3 deletions src/cublas.gemm.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -6,7 +6,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle, cublasOperation_t transa,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int cutoff_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUTOFF_THRESHOLD_ENV_NAME, false);
const int cutoff_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUTOFF_THRESHOLD_ENV_NAME, false);
if (cutoff_flag) {
double threshold;
try {
Expand All @@ -22,7 +22,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle, cublasOperation_t transa,
}
}

const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasOperation_t, cublasOperation_t, int, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, const CULIP_TYPE*, CULIP_TYPE*, int);
Expand Down Expand Up @@ -54,7 +54,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle, cublasOperation_t transa,
CULiP_launch_function(cuda_stream, &CULiP_print_profile_result, (void*)&profile_result);
}

const int exp_stats_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_EXP_STATS_ENABLE_ENV_NAME, false);
const int exp_stats_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_EXP_STATS_ENABLE_ENV_NAME, false);
if (exp_stats_flag) {
cudaStream_t cuda_stream;
cublasGetStream(handle, &cuda_stream);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.gemm_batched.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -16,7 +16,7 @@ cublasStatus_t CULIP_FUNC_NAME (cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasOperation_t, cublasOperation_t, int, int, int, const CULIP_TYPE* const, const CULIP_TYPE*const [], int, const CULIP_TYPE* const[], int, const CULIP_TYPE* const, CULIP_TYPE* const[], int, int);
Expand Down
6 changes: 3 additions & 3 deletions src/cublas.gemm_strided_batched.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -19,7 +19,7 @@ cublasStatus_t CULIP_FUNC_NAME (cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int cutoff_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUTOFF_THRESHOLD_ENV_NAME, false);
const int cutoff_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUTOFF_THRESHOLD_ENV_NAME, false);
if (cutoff_flag) {
double threshold;
try {
Expand All @@ -37,7 +37,7 @@ cublasStatus_t CULIP_FUNC_NAME (cublasHandle_t handle,
}
}

const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasOperation_t, cublasOperation_t, int, int, int, const CULIP_TYPE* const, const CULIP_TYPE*, int, long long int, const CULIP_TYPE*, int, long long int, const CULIP_TYPE* const, CULIP_TYPE*, int, long long int, int);
Expand Down Expand Up @@ -69,7 +69,7 @@ cublasStatus_t CULIP_FUNC_NAME (cublasHandle_t handle,
CULiP_launch_function(cuda_stream, &CULiP_print_profile_result, (void*)&profile_result);
}

const int exp_stats_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_EXP_STATS_ENABLE_ENV_NAME, false);
const int exp_stats_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_EXP_STATS_ENABLE_ENV_NAME, false);
if (exp_stats_flag) {
cudaStream_t cuda_stream;
cublasGetStream(handle, &cuda_stream);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.gemv.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -6,7 +6,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasOperation_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, const CULIP_TYPE*, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.ger.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -8,7 +8,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.hemm.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -7,7 +7,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasSideMode_t, cublasFillMode_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, const CULIP_TYPE*, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.her2k.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -9,7 +9,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasFillMode_t, cublasOperation_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, const CULIP_REAL_TYPE*, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.herk.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -6,7 +6,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasFillMode_t, cublasOperation_t, int, int, const CULIP_REAL_TYPE*, const CULIP_TYPE*, int, const CULIP_REAL_TYPE*, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.sbmv.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -6,7 +6,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasFillMode_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, const CULIP_TYPE*, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.spmv.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -6,7 +6,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasFillMode_t, int, const CULIP_TYPE*, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.symm.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -6,7 +6,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle, cublasSideMode_t side,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasSideMode_t, cublasFillMode_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, const CULIP_TYPE*, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.syr2k.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -9,7 +9,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasFillMode_t, cublasOperation_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, const CULIP_TYPE*, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.syrk.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -7,7 +7,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasFillMode_t, cublasOperation_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.trmm.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -9,7 +9,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasSideMode_t, cublasFillMode_t, cublasOperation_t, cublasDiagType_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, const CULIP_TYPE*, int, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.trsm.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -8,7 +8,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasSideMode_t, cublasFillMode_t, cublasOperation_t, cublasDiagType_t, int, int, const CULIP_TYPE*, const CULIP_TYPE*, int, CULIP_TYPE*, int);
Expand Down
2 changes: 1 addition & 1 deletion src/cublas.trsmBatched.template.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -9,7 +9,7 @@ cublasStatus_t CULIP_FUNC_NAME(cublasHandle_t handle,
#ifdef __CUDA_ARCH__
return CUBLAS_STATUS_NOT_SUPPORTED;
#else
const int profiling_flag = (CULiP_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);
const int profiling_flag = (CULiP_cublas_profiling_control_array[CULIP_FUNC_ENUM_NAME] == 0) && CULiP_is_profiling_enabled(CULIP_CUBLAS_DISABLE_ENV_NAME);

// Get the function pointer
cublasStatus_t (*cublas_lib_func)(cublasHandle_t, cublasSideMode_t, cublasFillMode_t, cublasOperation_t, cublasDiagType_t, int, int, const CULIP_TYPE*, const CULIP_TYPE *const [], int, CULIP_TYPE *const [], int, int);
Expand Down

0 comments on commit e8fe4fa

Please sign in to comment.