Lines Matching refs:error
54 cl_int error = clWaitForEvents(n, evs); in wait_and_release() local
55 if (error == CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST) { in wait_and_release()
58 … error = clGetEventInfo(evs[i], CL_EVENT_COMMAND_EXECUTION_STATUS, sizeof(cl_int), &e, NULL); in wait_and_release()
59 test_error(error, "clGetEventInfo failed"); in wait_and_release()
66 test_error(error, "clWaitForEvents failed"); in wait_and_release()
69 error = clReleaseEvent(evs[i]); in wait_and_release()
70 test_error(error, "clReleaseEvent failed"); in wait_and_release()
94 cl_int error; in test_svm_migrate() local
96 …error = create_cl_objects(deviceID, &sources[0], &context, &program, &queues[0], &num_devices, CL_… in test_svm_migrate()
97 if (error) in test_svm_migrate()
105 error = clGetCommandQueueInfo(queues[0], CL_QUEUE_DEVICE, sizeof(did), (void *)&did, NULL); in test_svm_migrate()
106 test_error(error, "clGetCommandQueueInfo failed"); in test_svm_migrate()
109 error = clGetCommandQueueInfo(queues[0], CL_QUEUE_PROPERTIES, sizeof(cqp), &cqp, NULL); in test_svm_migrate()
110 test_error(error, "clGetCommandQueueInfo failed"); in test_svm_migrate()
113 queues[1] = clCreateCommandQueueWithProperties(context, did, qp, &error); in test_svm_migrate()
114 test_error(error, "clCteateCommandQueueWithProperties failed"); in test_svm_migrate()
117 clKernelWrapper kernel = clCreateKernel(program, "migrate_kernel", &error); in test_svm_migrate()
118 test_error(error, "clCreateKernel failed"); in test_svm_migrate()
141 error = clSetKernelArgSVMPointer(kernel, 0, (void*)asvm); in test_svm_migrate()
142 test_error(error, "clSetKernelArgSVMPointer failed"); in test_svm_migrate()
144 error = clSetKernelArgSVMPointer(kernel, 1, (void*)bsvm); in test_svm_migrate()
145 test_error(error, "clSetKernelArgSVMPointer failed"); in test_svm_migrate()
147 error = clSetKernelArgSVMPointer(kernel, 2, (void*)csvm); in test_svm_migrate()
148 test_error(error, "clSetKernelArgSVMPointer failed"); in test_svm_migrate()
159 …error = clEnqueueSVMMemFill(queues[0], (void *)asvm, patt, sizeof(patt), global_size*sizeof(cl_uin… in test_svm_migrate()
160 test_error(error, "clEnqueueSVMMemFill failed"); in test_svm_migrate()
162 …error = clEnqueueSVMMemFill(queues[0], (void *)bsvm, patt, sizeof(patt), global_size*sizeof(cl_uin… in test_svm_migrate()
163 test_error(error, "clEnqueueSVMMemFill failed"); in test_svm_migrate()
165 …error = clEnqueueSVMMemFill(queues[0], (void *)csvm, patt, sizeof(patt), global_size*sizeof(cl_uin… in test_svm_migrate()
166 test_error(error, "clEnqueueSVMMemFill failed"); in test_svm_migrate()
172 …error = clEnqueueSVMMigrateMem(queues[1], 3, (const void**)ptrs, NULL, CL_MIGRATE_MEM_OBJECT_CONTE… in test_svm_migrate()
173 test_error(error, "clEnqueueSVMMigrateMem failed"); in test_svm_migrate()
180 …error = clEnqueueSVMMigrateMem(queues[0], 3, (const void**)ptrs, szs, CL_MIGRATE_MEM_OBJECT_HOST, … in test_svm_migrate()
181 test_error(error, "clEnqueueSVMMigrateMem failed"); in test_svm_migrate()
186 …error = clEnqueueSVMMap(queues[1], CL_FALSE, CL_MAP_WRITE, (void*)asvm, global_size*sizeof(cl_uint… in test_svm_migrate()
187 test_error(error, "clEnqueueSVMMap failed"); in test_svm_migrate()
189 …error = clEnqueueSVMMap(queues[1], CL_FALSE, CL_MAP_WRITE, (void*)bsvm, global_size*sizeof(cl_uint… in test_svm_migrate()
190 test_error(error, "clEnqueueSVMMap failed"); in test_svm_migrate()
192 …error = clEnqueueSVMMap(queues[1], CL_FALSE, CL_MAP_WRITE, (void*)csvm, global_size*sizeof(cl_uint… in test_svm_migrate()
193 test_error(error, "clEnqueueSVMMap failed"); in test_svm_migrate()
196 error = clFlush(queues[0]); in test_svm_migrate()
197 test_error(error, "clFlush failed"); in test_svm_migrate()
199 error = clFlush(queues[1]); in test_svm_migrate()
200 test_error(error, "clFlush failed"); in test_svm_migrate()
202 error = wait_and_release("first batch", evs, 8); in test_svm_migrate()
203 if (error) in test_svm_migrate()
211 error = clEnqueueSVMUnmap(queues[1], (void *)asvm, 0, NULL, &evs[0]); in test_svm_migrate()
212 test_error(error, "clEnqueueSVMUnmap failed"); in test_svm_migrate()
214 error = clEnqueueSVMUnmap(queues[1], (void *)bsvm, 0, NULL, &evs[1]); in test_svm_migrate()
215 test_error(error, "clEnqueueSVMUnmap failed"); in test_svm_migrate()
217 error = clEnqueueSVMUnmap(queues[1], (void *)csvm, 0, NULL, &evs[2]); in test_svm_migrate()
218 test_error(error, "clEnqueueSVMUnmap failed"); in test_svm_migrate()
227 … error = clEnqueueSVMMigrateMem(queues[0], 3, (const void**)ptrs, szs, 0, 1, &evs[2], &evs[3]); in test_svm_migrate()
228 test_error(error, "clEnqueueSVMMigrateMem failed"); in test_svm_migrate()
230 … error = clEnqueueNDRangeKernel(queues[0], kernel, 1, NULL, &global_size, NULL, 0, NULL, &evs[4]); in test_svm_migrate()
231 test_error(error, "clEnqueueNDRangeKernel failed"); in test_svm_migrate()
239 … error = clEnqueueSVMMigrateMem(queues[1], 4, (const void**)ptrs, szs, 0, 1, &evs[4], &evs[5]); in test_svm_migrate()
240 test_error(error, "clEnqueueSVMMigrateMem failed"); in test_svm_migrate()
242 … error = clEnqueueNDRangeKernel(queues[1], kernel, 1, NULL, &global_size, NULL, 0, NULL, &evs[6]); in test_svm_migrate()
243 test_error(error, "clEnqueueNDRangeKernel failed"); in test_svm_migrate()
251 … error = clEnqueueSVMMigrateMem(queues[0], 6, (const void**)ptrs, szs, 0, 1, &evs[6], &evs[7]); in test_svm_migrate()
252 test_error(error, "clEnqueueSVMMigrateMem failed"); in test_svm_migrate()
254 … error = clEnqueueNDRangeKernel(queues[0], kernel, 1, NULL, &global_size, NULL, 0, NULL, &evs[8]); in test_svm_migrate()
255 test_error(error, "clEnqueueNDRangeKernel failed"); in test_svm_migrate()
263 … error = clEnqueueSVMMigrateMem(queues[1], 5, (const void**)ptrs, szs, 0, 1, &evs[8], &evs[9]); in test_svm_migrate()
264 test_error(error, "clEnqueueSVMMigrateMem failed"); in test_svm_migrate()
266 … error = clEnqueueNDRangeKernel(queues[1], kernel, 1, NULL, &global_size, NULL, 0, NULL, &evs[10]); in test_svm_migrate()
267 test_error(error, "clEnqueueNDRangeKernel failed"); in test_svm_migrate()
271 …error = clEnqueueSVMMap(queues[1], CL_FALSE, CL_MAP_READ, (void*)asvm, global_size*sizeof(cl_uint)… in test_svm_migrate()
272 test_error(error, "clEnqueueSVMMap failed"); in test_svm_migrate()
274 …error = clEnqueueSVMMap(queues[1], CL_FALSE, CL_MAP_READ, (void*)bsvm, global_size*sizeof(cl_uint)… in test_svm_migrate()
275 test_error(error, "clEnqueueSVMMap failed"); in test_svm_migrate()
277 …error = clEnqueueSVMMap(queues[1], CL_FALSE, CL_MAP_READ, (void*)csvm, global_size*sizeof(cl_uint)… in test_svm_migrate()
278 test_error(error, "clEnqueueSVMMap failed"); in test_svm_migrate()
281 error = clFlush(queues[0]); in test_svm_migrate()
282 test_error(error, "clFlush failed"); in test_svm_migrate()
284 error = clFlush(queues[1]); in test_svm_migrate()
285 test_error(error, "clFlush failed"); in test_svm_migrate()
287 error = wait_and_release("batch 2", evs, 14); in test_svm_migrate()
288 if (error) in test_svm_migrate()
299 error = clEnqueueSVMUnmap(queues[1], (void *)asvm, 0, NULL, &evs[0]); in test_svm_migrate()
300 test_error(error, "clEnqueueSVMUnmap failed"); in test_svm_migrate()
302 error = clEnqueueSVMUnmap(queues[1], (void *)bsvm, 0, NULL, &evs[1]); in test_svm_migrate()
303 test_error(error, "clEnqueueSVMUnmap failed"); in test_svm_migrate()
305 error = clEnqueueSVMUnmap(queues[1], (void *)csvm, 0, NULL, &evs[2]); in test_svm_migrate()
306 test_error(error, "clEnqueueSVMUnmap failed"); in test_svm_migrate()
308 error = clEnqueueSVMFree(queues[1], 3, ptrs, NULL, NULL, 0, NULL, &evs[3]); in test_svm_migrate()
311 error = clFlush(queues[1]); in test_svm_migrate()
312 test_error(error, "clFlush failed"); in test_svm_migrate()
314 error = wait_and_release("batch 3", evs, 4); in test_svm_migrate()
315 if (error) in test_svm_migrate()