Skip to content
Navigation Menu
{{ message }}
forked from arrayfire/arrayfire-python
-
Notifications
You must be signed in to change notification settings - Fork 0
Expand file tree
/
Copy pathinterop.py
More file actions
302 lines (245 loc) · 9.04 KB
/
interop.py
File metadata and controls
302 lines (245 loc) · 9.04 KB
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
134
135
136
137
138
139
140
141
142
143
144
145
146
147
148
149
150
151
152
153
154
155
156
157
158
159
160
161
162
163
164
165
166
167
168
169
170
171
172
173
174
175
176
177
178
179
180
181
182
183
184
185
186
187
188
189
190
191
192
193
194
195
196
197
198
199
200
201
202
203
204
205
206
207
208
209
210
211
212
213
214
215
216
217
218
219
220
221
222
223
224
225
226
227
228
229
230
231
232
233
234
235
236
237
238
239
240
241
242
243
244
245
246
247
248
249
250
251
252
253
254
255
256
257
258
259
260
261
262
263
264
265
266
267
268
269
270
271
272
273
274
275
276
277
278
279
280
281
282
283
284
285
286
287
288
289
290
291
292
293
294
295
296
297
298
299
300
301
302
#######################################################
# Copyright (c) 2015, ArrayFire
# All rights reserved.
#
# This file is distributed under 3-clause BSD license.
# The complete license agreement can be obtained at:
# http://arrayfire.com/licenses/BSD-3-Clause
########################################################
"""
Interop with other python packages.
This module provides helper functions to copy data to arrayfire from the following modules:
1. numpy - numpy.ndarray
2. pycuda - pycuda.gpuarray
3. pyopencl - pyopencl.array
4. numba - numba.cuda.cudadrv.devicearray.DeviceNDArray
"""
from .array import *
from .device import *
def _fc_to_af_array(in_ptr, in_shape, in_dtype, is_device=False, copy = True):
"""
Fortran Contiguous to af array
"""
res = Array(in_ptr, in_shape, in_dtype, is_device=is_device)
if is_device:
lock_array(res)
pass
return res.copy() if copy else res
def _cc_to_af_array(in_ptr, ndim, in_shape, in_dtype, is_device=False, copy = True):
"""
C Contiguous to af array
"""
if ndim == 1:
return _fc_to_af_array(in_ptr, in_shape, in_dtype, is_device, copy)
elif ndim == 2:
shape = (in_shape[1], in_shape[0])
res = Array(in_ptr, shape, in_dtype, is_device=is_device)
if is_device: lock_array(res)
return reorder(res, 1, 0)
elif ndim == 3:
shape = (in_shape[2], in_shape[1], in_shape[0])
res = Array(in_ptr, shape, in_dtype, is_device=is_device)
if is_device: lock_array(res)
return reorder(res, 2, 1, 0)
elif ndim == 4:
shape = (in_shape[3], in_shape[2], in_shape[1], in_shape[0])
res = Array(in_ptr, shape, in_dtype, is_device=is_device)
if is_device: lock_array(res)
return reorder(res, 3, 2, 1, 0)
else:
raise RuntimeError("Unsupported ndim")
_nptype_to_aftype = {'b1' : Dtype.b8,
'u1' : Dtype.u8,
'u2' : Dtype.u16,
'i2' : Dtype.s16,
's4' : Dtype.u32,
'i4' : Dtype.s32,
'f4' : Dtype.f32,
'c8' : Dtype.c32,
's8' : Dtype.u64,
'i8' : Dtype.s64,
'f8' : Dtype.f64,
'c16' : Dtype.c64}
try:
import numpy as np
from numpy import ndarray as NumpyArray
from .data import reorder
AF_NUMPY_FOUND=True
def np_to_af_array(np_arr, copy=True):
"""
Convert numpy.ndarray to arrayfire.Array.
Parameters
----------
np_arr : numpy.ndarray()
copy : Bool specifying if array is to be copied.
Default is true.
Can only be False if array is fortran contiguous.
Returns
---------
af_arr : arrayfire.Array()
"""
in_shape = np_arr.shape
in_ptr = np_arr.ctypes.data_as(c_void_ptr_t)
in_dtype = _nptype_to_aftype[np_arr.dtype.str[1:]]
if not copy:
raise RuntimeError("Copy can not be False for numpy arrays")
if (np_arr.flags['F_CONTIGUOUS']):
return _fc_to_af_array(in_ptr, in_shape, in_dtype)
elif (np_arr.flags['C_CONTIGUOUS']):
return _cc_to_af_array(in_ptr, np_arr.ndim, in_shape, in_dtype)
else:
return np_to_af_array(np_arr.copy())
from_ndarray = np_to_af_array
except:
AF_NUMPY_FOUND=False
try:
import pycuda.gpuarray
from pycuda.gpuarray import GPUArray as CudaArray
AF_PYCUDA_FOUND=True
def pycuda_to_af_array(pycu_arr, copy=True):
"""
Convert pycuda.gpuarray to arrayfire.Array
Parameters
-----------
pycu_arr : pycuda.GPUArray()
copy : Bool specifying if array is to be copied.
Default is true.
Can only be False if array is fortran contiguous.
Returns
----------
af_arr : arrayfire.Array()
Note
----------
The input array is copied to af.Array
"""
in_ptr = pycu_arr.ptr
in_shape = pycu_arr.shape
in_dtype = pycu_arr.dtype.char
if not copy and not pycu_arr.flags.f_contiguous:
raise RuntimeError("Copy can only be False when arr.flags.f_contiguous is True")
if (pycu_arr.flags.f_contiguous):
return _fc_to_af_array(in_ptr, in_shape, in_dtype, True, copy)
elif (pycu_arr.flags.c_contiguous):
return _cc_to_af_array(in_ptr, pycu_arr.ndim, in_shape, in_dtype, True, copy)
else:
return pycuda_to_af_array(pycu_arr.copy())
except:
AF_PYCUDA_FOUND=False
try:
from pyopencl.array import Array as OpenclArray
from .opencl import add_device_context as _add_device_context
from .opencl import set_device_context as _set_device_context
from .opencl import get_device_id as _get_device_id
from .opencl import get_context as _get_context
AF_PYOPENCL_FOUND=True
def pyopencl_to_af_array(pycl_arr, copy=True):
"""
Convert pyopencl.gpuarray to arrayfire.Array
Parameters
-----------
pycl_arr : pyopencl.Array()
copy : Bool specifying if array is to be copied.
Default is true.
Can only be False if array is fortran contiguous.
Returns
----------
af_arr : arrayfire.Array()
Note
----------
The input array is copied to af.Array
"""
ctx = pycl_arr.context.int_ptr
que = pycl_arr.queue.int_ptr
dev = pycl_arr.queue.device.int_ptr
dev_idx = None
ctx_idx = None
for n in range(get_device_count()):
set_device(n)
dev_idx = _get_device_id()
ctx_idx = _get_context()
if (dev_idx == dev and ctx_idx == ctx):
break
if (dev_idx == None or ctx_idx == None or
dev_idx != dev or ctx_idx != ctx):
print("Adding context and queue")
_add_device_context(dev, ctx, que)
_set_device_context(dev, ctx)
info()
in_ptr = pycl_arr.base_data.int_ptr
in_shape = pycl_arr.shape
in_dtype = pycl_arr.dtype.char
if not copy and not pycl_arr.flags.f_contiguous:
raise RuntimeError("Copy can only be False when arr.flags.f_contiguous is True")
print("Copying array")
print(pycl_arr.base_data.int_ptr)
if (pycl_arr.flags.f_contiguous):
return _fc_to_af_array(in_ptr, in_shape, in_dtype, True, copy)
elif (pycl_arr.flags.c_contiguous):
return _cc_to_af_array(in_ptr, pycl_arr.ndim, in_shape, in_dtype, True, copy)
else:
return pyopencl_to_af_array(pycl_arr.copy())
except:
AF_PYOPENCL_FOUND=False
try:
import numba
from numba import cuda
NumbaCudaArray = cuda.cudadrv.devicearray.DeviceNDArray
AF_NUMBA_FOUND=True
def numba_to_af_array(nb_arr, copy=True):
"""
Convert numba.gpuarray to arrayfire.Array
Parameters
-----------
nb_arr : numba.cuda.cudadrv.devicearray.DeviceNDArray()
copy : Bool specifying if array is to be copied.
Default is true.
Can only be False if array is fortran contiguous.
Returns
----------
af_arr : arrayfire.Array()
Note
----------
The input array is copied to af.Array
"""
in_ptr = nb_arr.device_ctypes_pointer.value
in_shape = nb_arr.shape
in_dtype = _nptype_to_aftype[nb_arr.dtype.str[1:]]
if not copy and not nb_arr.flags.f_contiguous:
raise RuntimeError("Copy can only be False when arr.flags.f_contiguous is True")
if (nb_arr.is_f_contiguous()):
return _fc_to_af_array(in_ptr, in_shape, in_dtype, True, copy)
elif (nb_arr.is_c_contiguous()):
return _cc_to_af_array(in_ptr, nb_arr.ndim, in_shape, in_dtype, True, copy)
else:
return numba_to_af_array(nb_arr.copy())
except:
AF_NUMBA_FOUND=False
def to_array(in_array, copy = True):
"""
Helper function to convert input from a different module to af.Array
Parameters
-------------
in_array : array like object
Can be one of the following:
- numpy.ndarray
- pycuda.GPUArray
- pyopencl.Array
- numba.cuda.cudadrv.devicearray.DeviceNDArray
- array.array
- list
copy : Bool specifying if array is to be copied.
Default is true.
Can only be False if array is fortran contiguous.
Returns
--------------
af.Array of same dimensions as input after copying the data from the input
"""
if AF_NUMPY_FOUND and isinstance(in_array, NumpyArray):
return np_to_af_array(in_array, copy)
if AF_PYCUDA_FOUND and isinstance(in_array, CudaArray):
return pycuda_to_af_array(in_array, copy)
if AF_PYOPENCL_FOUND and isinstance(in_array, OpenclArray):
return pyopencl_to_af_array(in_array, copy)
if AF_NUMBA_FOUND and isinstance(in_array, NumbaCudaArray):
return numba_to_af_array(in_array, copy)
return Array(src=in_array)
You can’t perform that action at this time.