Mentions légales du service

Skip to content
Snippets Groups Projects
Commit f41be856 authored by Mathieu Faverge's avatar Mathieu Faverge
Browse files

Setting the kernel is done in the codelet

parent 117a67f9
No related branches found
No related tags found
1 merge request!36Starpu/cublas v2
...@@ -34,10 +34,6 @@ int CUDA_zgemm(MORSE_enum transa, MORSE_enum transb, ...@@ -34,10 +34,6 @@ int CUDA_zgemm(MORSE_enum transa, MORSE_enum transb,
cuDoubleComplex *C, int ldc, cuDoubleComplex *C, int ldc,
CUBLAS_STREAM_PARAM) CUBLAS_STREAM_PARAM)
{ {
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
cublasZgemm(CUBLAS_HANDLE cublasZgemm(CUBLAS_HANDLE
morse_lapack_const(transa), morse_lapack_const(transb), morse_lapack_const(transa), morse_lapack_const(transb),
m, n, k, m, n, k,
...@@ -46,6 +42,5 @@ int CUDA_zgemm(MORSE_enum transa, MORSE_enum transb, ...@@ -46,6 +42,5 @@ int CUDA_zgemm(MORSE_enum transa, MORSE_enum transb,
CUBLAS_VALUE(beta), C, ldc); CUBLAS_VALUE(beta), C, ldc);
assert( CUBLAS_STATUS_SUCCESS == cublasGetError() ); assert( CUBLAS_STATUS_SUCCESS == cublasGetError() );
return MORSE_SUCCESS; return MORSE_SUCCESS;
} }
...@@ -34,10 +34,6 @@ int CUDA_zhemm(MORSE_enum side, MORSE_enum uplo, ...@@ -34,10 +34,6 @@ int CUDA_zhemm(MORSE_enum side, MORSE_enum uplo,
cuDoubleComplex *C, int ldc, cuDoubleComplex *C, int ldc,
CUBLAS_STREAM_PARAM) CUBLAS_STREAM_PARAM)
{ {
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
cublasZhemm(CUBLAS_HANDLE cublasZhemm(CUBLAS_HANDLE
morse_lapack_const(side), morse_lapack_const(uplo), morse_lapack_const(side), morse_lapack_const(uplo),
m, n, m, n,
...@@ -46,6 +42,5 @@ int CUDA_zhemm(MORSE_enum side, MORSE_enum uplo, ...@@ -46,6 +42,5 @@ int CUDA_zhemm(MORSE_enum side, MORSE_enum uplo,
CUBLAS_VALUE(beta), C, ldc); CUBLAS_VALUE(beta), C, ldc);
assert( CUBLAS_STATUS_SUCCESS == cublasGetError() ); assert( CUBLAS_STATUS_SUCCESS == cublasGetError() );
return MORSE_SUCCESS; return MORSE_SUCCESS;
} }
...@@ -34,10 +34,6 @@ int CUDA_zher2k(MORSE_enum uplo, MORSE_enum trans, ...@@ -34,10 +34,6 @@ int CUDA_zher2k(MORSE_enum uplo, MORSE_enum trans,
cuDoubleComplex *C, int ldc, cuDoubleComplex *C, int ldc,
CUBLAS_STREAM_PARAM) CUBLAS_STREAM_PARAM)
{ {
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
cublasZher2k(CUBLAS_HANDLE cublasZher2k(CUBLAS_HANDLE
morse_lapack_const(uplo), morse_lapack_const(trans), morse_lapack_const(uplo), morse_lapack_const(trans),
n, k, n, k,
......
...@@ -33,10 +33,6 @@ int CUDA_zherk( MORSE_enum uplo, MORSE_enum trans, ...@@ -33,10 +33,6 @@ int CUDA_zherk( MORSE_enum uplo, MORSE_enum trans,
cuDoubleComplex *B, int ldb, cuDoubleComplex *B, int ldb,
CUBLAS_STREAM_PARAM) CUBLAS_STREAM_PARAM)
{ {
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
cublasZherk( cublasZherk(
morse_lapack_const(uplo), morse_lapack_const(trans), morse_lapack_const(uplo), morse_lapack_const(trans),
n, k, n, k,
......
...@@ -49,10 +49,6 @@ CUDA_zlarfb(MORSE_enum side, MORSE_enum trans, ...@@ -49,10 +49,6 @@ CUDA_zlarfb(MORSE_enum side, MORSE_enum trans,
MORSE_enum transT, uplo, notransV, transV; MORSE_enum transT, uplo, notransV, transV;
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
/* Check input arguments */ /* Check input arguments */
if ((side != MorseLeft) && (side != MorseRight)) { if ((side != MorseLeft) && (side != MorseRight)) {
return -1; return -1;
......
...@@ -34,10 +34,6 @@ int CUDA_zsymm(MORSE_enum side, MORSE_enum uplo, ...@@ -34,10 +34,6 @@ int CUDA_zsymm(MORSE_enum side, MORSE_enum uplo,
cuDoubleComplex *C, int ldc, cuDoubleComplex *C, int ldc,
CUBLAS_STREAM_PARAM) CUBLAS_STREAM_PARAM)
{ {
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
cublasZsymm(CUBLAS_HANDLE cublasZsymm(CUBLAS_HANDLE
morse_lapack_const(side), morse_lapack_const(uplo), morse_lapack_const(side), morse_lapack_const(uplo),
m, n, m, n,
......
...@@ -35,10 +35,6 @@ int CUDA_zsyr2k( ...@@ -35,10 +35,6 @@ int CUDA_zsyr2k(
cuDoubleComplex *C, int ldc, cuDoubleComplex *C, int ldc,
CUBLAS_STREAM_PARAM) CUBLAS_STREAM_PARAM)
{ {
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
cublasZsyr2k(CUBLAS_HANDLE cublasZsyr2k(CUBLAS_HANDLE
morse_lapack_const(uplo), morse_lapack_const(trans), morse_lapack_const(uplo), morse_lapack_const(trans),
n, k, n, k,
......
...@@ -33,10 +33,6 @@ int CUDA_zsyrk(MORSE_enum uplo, MORSE_enum trans, ...@@ -33,10 +33,6 @@ int CUDA_zsyrk(MORSE_enum uplo, MORSE_enum trans,
cuDoubleComplex *C, int ldc, cuDoubleComplex *C, int ldc,
CUBLAS_STREAM_PARAM) CUBLAS_STREAM_PARAM)
{ {
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
cublasZsyrk(CUBLAS_HANDLE cublasZsyrk(CUBLAS_HANDLE
morse_lapack_const(uplo), morse_lapack_const(trans), morse_lapack_const(uplo), morse_lapack_const(trans),
n, k, n, k,
......
...@@ -34,10 +34,6 @@ int CUDA_ztrmm( ...@@ -34,10 +34,6 @@ int CUDA_ztrmm(
cuDoubleComplex *B, int ldb, cuDoubleComplex *B, int ldb,
CUBLAS_STREAM_PARAM) CUBLAS_STREAM_PARAM)
{ {
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
cublasZtrmm(CUBLAS_HANDLE cublasZtrmm(CUBLAS_HANDLE
morse_lapack_const(side), morse_lapack_const(uplo), morse_lapack_const(side), morse_lapack_const(uplo),
morse_lapack_const(transa), morse_lapack_const(diag), morse_lapack_const(transa), morse_lapack_const(diag),
......
...@@ -33,10 +33,6 @@ int CUDA_ztrsm(MORSE_enum side, MORSE_enum uplo, ...@@ -33,10 +33,6 @@ int CUDA_ztrsm(MORSE_enum side, MORSE_enum uplo,
cuDoubleComplex *B, int ldb, cuDoubleComplex *B, int ldb,
CUBLAS_STREAM_PARAM) CUBLAS_STREAM_PARAM)
{ {
#if !defined(CHAMELEON_USE_CUBLAS_V2)
cublasSetKernelStream( stream );
#endif
cublasZtrsm(CUBLAS_HANDLE cublasZtrsm(CUBLAS_HANDLE
morse_lapack_const(side), morse_lapack_const(uplo), morse_lapack_const(side), morse_lapack_const(uplo),
morse_lapack_const(transa), morse_lapack_const(diag), morse_lapack_const(transa), morse_lapack_const(diag),
......
0% Loading or .
You are about to add 0 people to the discussion. Proceed with caution.
Finish editing this message first!
Please register or to comment