Lines Matching refs:sycl_queue

65   if (!data->sycl_queue.is_in_order()) e = {data->sycl_queue.ext_oneapi_submit_barrier()};  in CeedVectorSyncH2D_Sycl()
66 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(impl->h_array, impl->d_array, length, e).wait… in CeedVectorSyncH2D_Sycl()
99 if (!data->sycl_queue.is_in_order()) e = {data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedVectorSyncD2H_Sycl()
100 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(impl->d_array, impl->h_array, length, e).wait… in CeedVectorSyncD2H_Sycl()
215 if (!data->sycl_queue.is_in_order()) e = {data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedVectorSetArrayDevice_Sycl()
224 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(array, impl->d_array_owned, length, e).wait_a… in CeedVectorSetArrayDevice_Sycl()
232 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedVectorSetArrayDevice_Sycl()
242 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedVectorSetArrayDevice_Sycl()
284 static int CeedDeviceSetValue_Sycl(sycl::queue &sycl_queue, CeedScalar *d_array, CeedSize length, C… in CeedDeviceSetValue_Sycl() argument
287 if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()}; in CeedDeviceSetValue_Sycl()
288 sycl_queue.fill(d_array, val, length, e); in CeedDeviceSetValue_Sycl()
322 CeedCallBackend(CeedDeviceSetValue_Sycl(data->sycl_queue, impl->d_array, length, val)); in CeedVectorSetValue_Sycl()
347 if (!data->sycl_queue.is_in_order()) data->sycl_queue.ext_oneapi_submit_barrier(); in CeedVectorTakeArray_Sycl()
467 if (!data->sycl_queue.is_in_order()) e = {data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedVectorNorm_Sycl()
473 …data->sycl_queue.parallel_for(length, e, sumReduction, [=](sycl::id<1> i, auto &sum) { sum += abs(… in CeedVectorNorm_Sycl()
478 …data->sycl_queue.parallel_for(length, e, sumReduction, [=](sycl::id<1> i, auto &sum) { sum += (d_a… in CeedVectorNorm_Sycl()
483 …data->sycl_queue.parallel_for(length, e, maxReduction, [=](sycl::id<1> i, auto &max) { max.combine… in CeedVectorNorm_Sycl()
506 static int CeedDeviceReciprocal_Sycl(sycl::queue &sycl_queue, CeedScalar *d_array, CeedSize length)… in CeedDeviceReciprocal_Sycl() argument
509 if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()}; in CeedDeviceReciprocal_Sycl()
510 sycl_queue.parallel_for(length, e, [=](sycl::id<1> i) { in CeedDeviceReciprocal_Sycl()
532 …if (impl->d_array) CeedCallBackend(CeedDeviceReciprocal_Sycl(data->sycl_queue, impl->d_array, leng… in CeedVectorReciprocal_Sycl()
548 static int CeedDeviceScale_Sycl(sycl::queue &sycl_queue, CeedScalar *x_array, CeedScalar alpha, Cee… in CeedDeviceScale_Sycl() argument
551 if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()}; in CeedDeviceScale_Sycl()
552 sycl_queue.parallel_for(length, e, [=](sycl::id<1> i) { x_array[i] *= alpha; }); in CeedDeviceScale_Sycl()
572 …if (x_impl->d_array) CeedCallBackend(CeedDeviceScale_Sycl(data->sycl_queue, x_impl->d_array, alpha… in CeedVectorScale_Sycl()
588 static int CeedDeviceAXPY_Sycl(sycl::queue &sycl_queue, CeedScalar *y_array, CeedScalar alpha, Ceed… in CeedDeviceAXPY_Sycl() argument
591 if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()}; in CeedDeviceAXPY_Sycl()
592 sycl_queue.parallel_for(length, e, [=](sycl::id<1> i) { y_array[i] += alpha * x_array[i]; }); in CeedDeviceAXPY_Sycl()
615 …CeedCallBackend(CeedDeviceAXPY_Sycl(data->sycl_queue, y_impl->d_array, alpha, x_impl->d_array, len… in CeedVectorAXPY_Sycl()
635 static int CeedDevicePointwiseMult_Sycl(sycl::queue &sycl_queue, CeedScalar *w_array, CeedScalar *x… in CeedDevicePointwiseMult_Sycl() argument
638 if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()}; in CeedDevicePointwiseMult_Sycl()
639 sycl_queue.parallel_for(length, e, [=](sycl::id<1> i) { w_array[i] = x_array[i] * y_array[i]; }); in CeedDevicePointwiseMult_Sycl()
667 …CeedCallBackend(CeedDevicePointwiseMult_Sycl(data->sycl_queue, w_impl->d_array, x_impl->d_array, y… in CeedVectorPointwiseMult_Sycl()
690 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedVectorDestroy_Sycl()