-
Notifications
You must be signed in to change notification settings - Fork 1
Expand file tree
/
Copy pathdraft.py
More file actions
58 lines (47 loc) · 1.54 KB
/
Copy pathdraft.py
File metadata and controls
58 lines (47 loc) · 1.54 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
__author__ = "hervemarie-nelly"
import pycuda
import pycuda.driver as cuda
from pycuda.compiler import SourceModule
import multiprocessing
import numpy
class GPUProcess(multiprocessing.Process):
def __init__(self, number, some_array):
multiprocessing.Process.__init__(self)
self.number = number
self.some_array = some_array
def run(self):
cuda.init() # INITIALISE HERE
self.dev = cuda.Device(self.number)
self.ctx = self.dev.make_context()
self.array_gpu = cuda.mem_alloc(some_array.nbytes)
cuda.memcpy_htod(self.array_gpu, some_array)
test_kernel(self.array_gpu)
print("successful exit from thread %d" % self.number)
self.ctx.pop()
del self.array_gpu
del self.ctx
def test_kernel(input_array_gpu):
mod = SourceModule(
"""
__global__ void f(float * out, float * in)
{
int idx = threadIdx.x;
out[idx] = in[idx] + 6;
}
"""
)
func = mod.get_function("f")
output_array = numpy.zeros((1, 512))
output_array_gpu = cuda.mem_alloc(output_array.nbytes)
func(output_array_gpu, input_array_gpu, block=(512, 1, 1))
cuda.memcpy_dtoh(output_array, output_array_gpu)
return output_array
# cuda.init() #COMMENT HERE
some_array = numpy.ones((1, 512), dtype=numpy.float32)
# num = cuda.Device.count() #COMMENT HERE
num = 2
gpu_process_list = []
for i in range(num):
gpu_process = GPUProcess(i, some_array)
gpu_process.start()
gpu_process_list.append(gpu_process)