Lines Matching refs:d_array

31       *need_sync = has_valid_array && !impl->d_array;  in CeedVectorNeedSync_Sycl()
54 impl->d_array = impl->d_array_borrowed; in CeedVectorSyncH2D_Sycl()
56 impl->d_array = impl->d_array_owned; in CeedVectorSyncH2D_Sycl()
59 impl->d_array = impl->d_array_owned; in CeedVectorSyncH2D_Sycl()
66 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(impl->h_array, impl->d_array, length, e).wait… in CeedVectorSyncH2D_Sycl()
84 CeedCheck(impl->d_array, ceed, CEED_ERROR_BACKEND, "No valid device data to sync to host"); in CeedVectorSyncD2H_Sycl()
100 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(impl->d_array, impl->h_array, length, e).wait… in CeedVectorSyncD2H_Sycl()
132 impl->d_array = NULL; in CeedVectorSetAllInvalid_Sycl()
143 *has_valid_array = impl->h_array || impl->d_array; in CeedVectorHasValidArray_Sycl()
227 impl->d_array = impl->d_array_owned; in CeedVectorSetArrayDevice_Sycl()
237 impl->d_array = impl->d_array_owned; in CeedVectorSetArrayDevice_Sycl()
247 impl->d_array = impl->d_array_borrowed; in CeedVectorSetArrayDevice_Sycl()
284 static int CeedDeviceSetValue_Sycl(sycl::queue &sycl_queue, CeedScalar *d_array, CeedSize length, C… in CeedDeviceSetValue_Sycl() argument
288 sycl_queue.fill(d_array, val, length, e); in CeedDeviceSetValue_Sycl()
308 if (!impl->d_array && !impl->h_array) { in CeedVectorSetValue_Sycl()
310 impl->d_array = impl->d_array_borrowed; in CeedVectorSetValue_Sycl()
314 impl->d_array = impl->d_array_owned; in CeedVectorSetValue_Sycl()
321 if (impl->d_array) { in CeedVectorSetValue_Sycl()
322 CeedCallBackend(CeedDeviceSetValue_Sycl(data->sycl_queue, impl->d_array, length, val)); in CeedVectorSetValue_Sycl()
327 impl->d_array = NULL; in CeedVectorSetValue_Sycl()
362 impl->d_array = NULL; in CeedVectorTakeArray_Sycl()
386 *array = impl->d_array; in CeedVectorGetArrayCore_Sycl()
413 impl->d_array = *array; in CeedVectorGetArray_Sycl()
439 if (impl->d_array_borrowed) impl->d_array = impl->d_array_borrowed; in CeedVectorGetArrayWrite_Sycl()
440 else impl->d_array = impl->d_array_owned; in CeedVectorGetArrayWrite_Sycl()
453 const CeedScalar *d_array; in CeedVectorNorm_Sycl() local
463 CeedCallBackend(CeedVectorGetArrayRead(vec, CEED_MEM_DEVICE, &d_array)); in CeedVectorNorm_Sycl()
473 …_for(length, e, sumReduction, [=](sycl::id<1> i, auto &sum) { sum += abs(d_array[i]); }).wait_and_… in CeedVectorNorm_Sycl()
478 …(length, e, sumReduction, [=](sycl::id<1> i, auto &sum) { sum += (d_array[i] * d_array[i]); }).wai… in CeedVectorNorm_Sycl()
483 …length, e, maxReduction, [=](sycl::id<1> i, auto &max) { max.combine(abs(d_array[i])); }).wait_and… in CeedVectorNorm_Sycl()
489 CeedCallBackend(CeedVectorRestoreArrayRead(vec, &d_array)); in CeedVectorNorm_Sycl()
506 static int CeedDeviceReciprocal_Sycl(sycl::queue &sycl_queue, CeedScalar *d_array, CeedSize length)… in CeedDeviceReciprocal_Sycl() argument
511 if (std::fabs(d_array[i]) > CEED_EPSILON) d_array[i] = 1. / d_array[i]; in CeedDeviceReciprocal_Sycl()
532 …if (impl->d_array) CeedCallBackend(CeedDeviceReciprocal_Sycl(data->sycl_queue, impl->d_array, leng… in CeedVectorReciprocal_Sycl()
572 …if (x_impl->d_array) CeedCallBackend(CeedDeviceScale_Sycl(data->sycl_queue, x_impl->d_array, alpha… in CeedVectorScale_Sycl()
613 if (y_impl->d_array) { in CeedVectorAXPY_Sycl()
615 …CeedCallBackend(CeedDeviceAXPY_Sycl(data->sycl_queue, y_impl->d_array, alpha, x_impl->d_array, len… in CeedVectorAXPY_Sycl()
661 if (!w_impl->d_array && !w_impl->h_array) { in CeedVectorPointwiseMult_Sycl()
664 if (w_impl->d_array) { in CeedVectorPointwiseMult_Sycl()
667 …(CeedDevicePointwiseMult_Sycl(data->sycl_queue, w_impl->d_array, x_impl->d_array, y_impl->d_array,… in CeedVectorPointwiseMult_Sycl()