1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
112
113
114
115
116
117
118
119
120
121
122
123
124
125
126
127
128
129
130
131
132
133
|
/*
-- MAGMA (version 2.9.0) --
Univ. of Tennessee, Knoxville
Univ. of California, Berkeley
Univ. of Colorado, Denver
@date January 2025
@author Mark Gates
*/
#ifndef MAGMA_NO_V1
#include "magma_internal.h"
#include "magmablas_v1.h" // includes v1 prototypes; does NOT map routine names
#include "error.h"
#include <cuda_runtime.h>
#if defined(MAGMA_HAVE_CUDA) || defined(MAGMA_HAVE_HIP)
// These MAGMA v1 routines are all deprecated.
// See copy_v2.cpp for documentation.
// Generic, type-independent routines to copy data.
// Type-safe versions which avoid the user needing sizeof(...) are in headers;
// see magma_{s,d,c,z,i,index_}{set,get,copy}{matrix,vector}
/******************************************************************************/
extern "C" void
magma_setvector_v1_internal(
magma_int_t n, magma_int_t elemSize,
void const* hx_src, magma_int_t incx,
magma_ptr dy_dst, magma_int_t incy,
const char* func, const char* file, int line )
{
magma_setvector_internal(
n, elemSize,
hx_src, incx,
dy_dst, incy,
magmablasGetQueue(),
func, file, line );
}
/******************************************************************************/
extern "C" void
magma_getvector_v1_internal(
magma_int_t n, magma_int_t elemSize,
magma_const_ptr dx_src, magma_int_t incx,
void* hy_dst, magma_int_t incy,
const char* func, const char* file, int line )
{
magma_getvector_internal(
n, elemSize,
dx_src, incx,
hy_dst, incy,
magmablasGetQueue(),
func, file, line );
}
/******************************************************************************/
extern "C" void
magma_copyvector_v1_internal(
magma_int_t n, magma_int_t elemSize,
magma_const_ptr dx_src, magma_int_t incx,
magma_ptr dy_dst, magma_int_t incy,
const char* func, const char* file, int line )
{
magma_copyvector_internal(
n, elemSize,
dx_src, incx,
dy_dst, incy,
magmablasGetQueue(),
func, file, line );
}
/******************************************************************************/
extern "C" void
magma_setmatrix_v1_internal(
magma_int_t m, magma_int_t n, magma_int_t elemSize,
void const* hA_src, magma_int_t lda,
magma_ptr dB_dst, magma_int_t lddb,
const char* func, const char* file, int line )
{
cublasStatus_t status;
status = cublasSetMatrix(
int(m), int(n), int(elemSize),
hA_src, int(lda),
dB_dst, int(lddb) );
check_xerror( status, func, file, line );
MAGMA_UNUSED( status );
}
/******************************************************************************/
extern "C" void
magma_getmatrix_v1_internal(
magma_int_t m, magma_int_t n, magma_int_t elemSize,
magma_const_ptr dA_src, magma_int_t ldda,
void* hB_dst, magma_int_t ldb,
const char* func, const char* file, int line )
{
cublasStatus_t status;
status = cublasGetMatrix(
int(m), int(n), int(elemSize),
dA_src, int(ldda),
hB_dst, int(ldb) );
check_xerror( status, func, file, line );
MAGMA_UNUSED( status );
}
/******************************************************************************/
extern "C" void
magma_copymatrix_v1_internal(
magma_int_t m, magma_int_t n, magma_int_t elemSize,
magma_const_ptr dA_src, magma_int_t ldda,
magma_ptr dB_dst, magma_int_t lddb,
const char* func, const char* file, int line )
{
cudaError_t status;
status = cudaMemcpy2D(
dB_dst, int(lddb*elemSize),
dA_src, int(ldda*elemSize),
int(m*elemSize), int(n), cudaMemcpyDeviceToDevice );
check_xerror( status, func, file, line );
MAGMA_UNUSED( status );
}
#endif // MAGMA_HAVE_CUDA
#endif // MAGMA_NO_V1
|
