Commit 57a4eb0f authored by PRUVOST Florent's avatar PRUVOST Florent

avoid using C99 feature - declarations should appear on top of functions

parent 52620b70
......@@ -193,13 +193,14 @@ static void cl_zhemm_cuda_func(void *descr[], void *cl_arg)
cuDoubleComplex beta;
cuDoubleComplex *C;
int LDC;
CUstream stream;
A = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
B = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
C = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[2]);
starpu_codelet_unpack_args(cl_arg, &side, &uplo, &M, &N, &alpha, &LDA, &LDB, &beta, &LDC);
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
cublasZhemm(
......
......@@ -187,13 +187,14 @@ static void cl_zher2k_cuda_func(void *descr[], void *cl_arg)
double beta;
cuDoubleComplex *C;
int ldc;
CUstream stream;
A = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
B = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
C = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[2]);
starpu_codelet_unpack_args(cl_arg, &uplo, &trans, &n, &k, &alpha, &lda, &ldb, &beta, &ldc);
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
cublasZher2k( morse_lapack_const(uplo), morse_lapack_const(trans),
......
......@@ -180,12 +180,13 @@ static void cl_zherk_cuda_func(void *descr[], void *cl_arg)
double beta;
cuDoubleComplex *C;
int ldc;
CUstream stream;
A = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
C = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
starpu_codelet_unpack_args(cl_arg, &uplo, &trans, &n, &k, &alpha, &lda, &beta, &ldc);
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
cublasZherk(
......
......@@ -193,13 +193,14 @@ static void cl_zsymm_cuda_func(void *descr[], void *cl_arg)
cuDoubleComplex beta;
cuDoubleComplex *C;
int LDC;
CUstream stream;
A = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
B = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
C = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[2]);
starpu_codelet_unpack_args(cl_arg, &side, &uplo, &M, &N, &alpha, &LDA, &LDB, &beta, &LDC);
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
cublasZsymm(
......
......@@ -187,13 +187,14 @@ static void cl_zsyr2k_cuda_func(void *descr[], void *cl_arg)
cuDoubleComplex beta;
cuDoubleComplex *C;
int ldc;
CUstream stream;
A = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
B = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
C = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[2]);
starpu_codelet_unpack_args(cl_arg, &uplo, &trans, &n, &k, &alpha, &lda, &ldb, &beta, &ldc);
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
cublasZsyr2k( morse_lapack_const(uplo), morse_lapack_const(trans),
......
......@@ -181,12 +181,13 @@ static void cl_zsyrk_cuda_func(void *descr[], void *cl_arg)
cuDoubleComplex beta;
cuDoubleComplex *C;
int ldc;
CUstream stream;
A = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
C = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
starpu_codelet_unpack_args(cl_arg, &uplo, &trans, &n, &k, &alpha, &lda, &beta, &ldc);
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
cublasZsyrk(
......
......@@ -202,12 +202,13 @@ static void cl_ztrmm_cuda_func(void *descr[], void *cl_arg)
int LDA;
cuDoubleComplex *B;
int LDB;
CUstream stream;
A = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
B = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
starpu_codelet_unpack_args(cl_arg, &side, &uplo, &transA, &diag, &M, &N, &alpha, &LDA, &LDB);
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
cublasZtrmm(
......
......@@ -202,12 +202,13 @@ static void cl_ztrsm_cuda_func(void *descr[], void *cl_arg)
int lda;
cuDoubleComplex *B;
int ldb;
CUstream stream;
A = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
B = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
starpu_codelet_unpack_args(cl_arg, &side, &uplo, &transA, &diag, &m, &n, &alpha, &lda, &ldb);
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
cublasZtrsm(
......
......@@ -333,6 +333,7 @@ static void cl_ztslqt_cuda_func(void *descr[], void *cl_arg)
cuDoubleComplex *h_A2, *h_T, *h_D, *h_TAU, *h_W;
cuDoubleComplex *d_A1, *d_A2, *d_T, *d_D, *d_W;
int lda1, lda2, ldt;
CUstream stream;
starpu_codelet_unpack_args(cl_arg, &m, &n, &ib, &lda1, &lda2, &ldt, &h_work);
......@@ -351,7 +352,7 @@ static void cl_ztslqt_cuda_func(void *descr[], void *cl_arg)
h_W = h_TAU + max(m,n);
h_D = h_W + ib*m;
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
magma_ztslqt_gpu( m, n, ib,
d_A1, lda1, d_A2, lda2,
h_A2, ib,
......
......@@ -363,6 +363,7 @@ static void cl_ztsmlq_cuda_func(void *descr[], void *cl_arg)
cuDoubleComplex *W, *WC;
int ldwork;
int ldworkc;
CUstream stream;
A1 = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
A2 = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
......@@ -376,7 +377,7 @@ static void cl_ztsmlq_cuda_func(void *descr[], void *cl_arg)
WC = W + ib * ldwork;
ldworkc = (side == MorseLeft) ? m1 : ib;
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
magma_ztsmlq_gpu( side, trans, m1, n1, m2, n2, k, ib,
......
......@@ -912,6 +912,7 @@ static void cl_ztsmqr_cuda_func(void *descr[], void *cl_arg)
cuDoubleComplex *W, *WC;
int ldwork;
int ldworkc;
CUstream stream;
A1 = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[0]);
A2 = (cuDoubleComplex *)STARPU_MATRIX_GET_PTR(descr[1]);
......@@ -925,7 +926,7 @@ static void cl_ztsmqr_cuda_func(void *descr[], void *cl_arg)
WC = W + ib * (side == MorseLeft ? n1 : m1);
ldworkc = (side == MorseLeft) ? m1 : ib;
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
cublasSetKernelStream( stream );
magma_ztsmqr_gpu( side, trans, m1, n1, m2, n2, k, ib,
......
......@@ -345,6 +345,7 @@ static void cl_ztsqrt_cuda_func(void *descr[], void *cl_arg)
cuDoubleComplex *h_A2, *h_T, *h_D, *h_TAU, *h_W;
cuDoubleComplex *d_A1, *d_A2, *d_T, *d_D, *d_W;
int lda1, lda2, ldt;
CUstream stream;
starpu_codelet_unpack_args(cl_arg, &m, &n, &ib, &lda1, &lda2, &ldt, &h_work);
......@@ -363,7 +364,7 @@ static void cl_ztsqrt_cuda_func(void *descr[], void *cl_arg)
h_W = h_TAU + max(m,n);
h_D = h_W + ib*n;
CUstream stream = starpu_cuda_get_local_stream();
stream = starpu_cuda_get_local_stream();
magma_ztsqrt2_gpu( m, n, ib,
d_A1, lda1, d_A2, lda2,
h_A2, lda2,
......
Markdown is supported
0% or .
You are about to add 0 people to the discussion. Proceed with caution.
Finish editing this message first!
Please register or to comment