Lines Matching refs:sycl
58 …CeedCallSycl(ceed, impl->d_array_owned = sycl::malloc_device<CeedScalar>(length, data->sycl_device… in CeedVectorSyncH2D_Sycl()
63 std::vector<sycl::event> e; in CeedVectorSyncH2D_Sycl()
97 std::vector<sycl::event> e; in CeedVectorSyncD2H_Sycl()
213 std::vector<sycl::event> e; in CeedVectorSetArrayDevice_Sycl()
220 …CeedCallSycl(ceed, impl->d_array_owned = sycl::malloc_device<CeedScalar>(length, data->sycl_device… in CeedVectorSetArrayDevice_Sycl()
233 CeedCallSycl(ceed, sycl::free(impl->d_array_owned, data->sycl_context)); in CeedVectorSetArrayDevice_Sycl()
243 CeedCallSycl(ceed, sycl::free(impl->d_array_owned, data->sycl_context)); in CeedVectorSetArrayDevice_Sycl()
284 static int CeedDeviceSetValue_Sycl(sycl::queue &sycl_queue, CeedScalar *d_array, CeedSize length, C… in CeedDeviceSetValue_Sycl()
285 std::vector<sycl::event> e; in CeedDeviceSetValue_Sycl()
465 std::vector<sycl::event> e; in CeedVectorNorm_Sycl()
472 …auto sumReduction = sycl::reduction(impl->reduction_norm, sycl::plus<>(), {sycl::property::reducti… in CeedVectorNorm_Sycl()
473 …data->sycl_queue.parallel_for(length, e, sumReduction, [=](sycl::id<1> i, auto &sum) { sum += abs(… in CeedVectorNorm_Sycl()
477 …auto sumReduction = sycl::reduction(impl->reduction_norm, sycl::plus<>(), {sycl::property::reducti… in CeedVectorNorm_Sycl()
478 …data->sycl_queue.parallel_for(length, e, sumReduction, [=](sycl::id<1> i, auto &sum) { sum += (d_a… in CeedVectorNorm_Sycl()
482 …auto maxReduction = sycl::reduction(impl->reduction_norm, sycl::maximum<>(), {sycl::property::redu… 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()
507 std::vector<sycl::event> e; in CeedDeviceReciprocal_Sycl()
510 sycl_queue.parallel_for(length, e, [=](sycl::id<1> i) { in CeedDeviceReciprocal_Sycl()
548 static int CeedDeviceScale_Sycl(sycl::queue &sycl_queue, CeedScalar *x_array, CeedScalar alpha, Cee… in CeedDeviceScale_Sycl()
549 std::vector<sycl::event> e; in CeedDeviceScale_Sycl()
552 sycl_queue.parallel_for(length, e, [=](sycl::id<1> i) { x_array[i] *= alpha; }); in CeedDeviceScale_Sycl()
588 static int CeedDeviceAXPY_Sycl(sycl::queue &sycl_queue, CeedScalar *y_array, CeedScalar alpha, Ceed… in CeedDeviceAXPY_Sycl()
589 std::vector<sycl::event> e; in CeedDeviceAXPY_Sycl()
592 sycl_queue.parallel_for(length, e, [=](sycl::id<1> i) { y_array[i] += alpha * x_array[i]; }); in CeedDeviceAXPY_Sycl()
635 static int CeedDevicePointwiseMult_Sycl(sycl::queue &sycl_queue, CeedScalar *w_array, CeedScalar *x… in CeedDevicePointwiseMult_Sycl()
636 std::vector<sycl::event> e; 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()
691 CeedCallSycl(ceed, sycl::free(impl->d_array_owned, data->sycl_context)); in CeedVectorDestroy_Sycl()
692 CeedCallSycl(ceed, sycl::free(impl->reduction_norm, data->sycl_context)); in CeedVectorDestroy_Sycl()
711 CeedCallSycl(ceed, impl->reduction_norm = sycl::malloc_host<CeedScalar>(1, data->sycl_context)); in CeedVectorCreate_Sycl()