Lines Matching refs:h_array
29 *need_sync = has_valid_array && !impl->h_array; in CeedVectorNeedSync_Cuda()
48 …CeedCheck(impl->h_array, CeedVectorReturnCeed(vec), CEED_ERROR_BACKEND, "No valid host data to syn… in CeedVectorSyncH2D_Cuda()
60 …CeedCallCuda(CeedVectorReturnCeed(vec), cudaMemcpy(impl->d_array, impl->h_array, bytes, cudaMemcpy… in CeedVectorSyncH2D_Cuda()
76 impl->h_array = impl->h_array_borrowed; in CeedVectorSyncD2H_Cuda()
78 impl->h_array = impl->h_array_owned; in CeedVectorSyncD2H_Cuda()
84 impl->h_array = impl->h_array_owned; in CeedVectorSyncD2H_Cuda()
90 …CeedCallCuda(CeedVectorReturnCeed(vec), cudaMemcpy(impl->h_array, impl->d_array, bytes, cudaMemcpy… in CeedVectorSyncD2H_Cuda()
120 impl->h_array = NULL; in CeedVectorSetAllInvalid_Cuda()
132 *has_valid_array = impl->h_array || impl->d_array; in CeedVectorHasValidArray_Cuda()
183 … (const CeedScalar **)&impl->h_array_borrowed, (const CeedScalar **)&impl->h_array)); in CeedVectorSetArrayHost_Cuda()
226 static int CeedHostCopyStrided_Cuda(CeedScalar *h_array, CeedSize start, CeedSize stop, CeedSize st… in CeedHostCopyStrided_Cuda() argument
227 for (CeedSize i = start; i < stop; i += step) h_copy_array[i] = h_array[i]; in CeedHostCopyStrided_Cuda()
273 impl->h_array = NULL; in CeedVectorCopyStrided_Cuda()
274 } else if (impl->h_array) { in CeedVectorCopyStrided_Cuda()
278 CeedCallBackend(CeedHostCopyStrided_Cuda(impl->h_array, start, stop, step, copy_array)); in CeedVectorCopyStrided_Cuda()
290 static int CeedHostSetValue_Cuda(CeedScalar *h_array, CeedSize length, CeedScalar val) { in CeedHostSetValue_Cuda() argument
291 for (CeedSize i = 0; i < length; i++) h_array[i] = val; in CeedHostSetValue_Cuda()
310 if (!impl->d_array && !impl->h_array) { in CeedVectorSetValue_Cuda()
314 impl->h_array = impl->h_array_borrowed; in CeedVectorSetValue_Cuda()
318 impl->h_array = impl->h_array_owned; in CeedVectorSetValue_Cuda()
329 impl->h_array = NULL; in CeedVectorSetValue_Cuda()
330 } else if (impl->h_array) { in CeedVectorSetValue_Cuda()
331 CeedCallBackend(CeedHostSetValue_Cuda(impl->h_array, length, val)); in CeedVectorSetValue_Cuda()
340 static int CeedHostSetValueStrided_Cuda(CeedScalar *h_array, CeedSize start, CeedSize stop, CeedSiz… in CeedHostSetValueStrided_Cuda() argument
341 for (CeedSize i = start; i < stop; i += step) h_array[i] = val; in CeedHostSetValueStrided_Cuda()
363 impl->h_array = NULL; in CeedVectorSetValueStrided_Cuda()
364 } else if (impl->h_array) { in CeedVectorSetValueStrided_Cuda()
365 CeedCallBackend(CeedHostSetValueStrided_Cuda(impl->h_array, start, stop, step, val)); in CeedVectorSetValueStrided_Cuda()
387 impl->h_array = NULL; in CeedVectorTakeArray_Cuda()
411 *array = impl->h_array; in CeedVectorGetArrayCore_Cuda()
438 impl->h_array = *array; in CeedVectorGetArray_Cuda()
463 if (impl->h_array_borrowed) impl->h_array = impl->h_array_borrowed; in CeedVectorGetArrayWrite_Cuda()
464 else impl->h_array = impl->h_array_owned; in CeedVectorGetArrayWrite_Cuda()
639 static int CeedHostReciprocal_Cuda(CeedScalar *h_array, CeedSize length) { in CeedHostReciprocal_Cuda() argument
641 if (fabs(h_array[i]) > CEED_EPSILON) h_array[i] = 1. / h_array[i]; in CeedHostReciprocal_Cuda()
662 if (impl->h_array) CeedCallBackend(CeedHostReciprocal_Cuda(impl->h_array, length)); in CeedVectorReciprocal_Cuda()
702 impl->h_array = NULL; in CeedVectorScale_Cuda()
703 } else if (impl->h_array) { in CeedVectorScale_Cuda()
704 CeedCallBackend(CeedHostScale_Cuda(impl->h_array, alpha, length)); in CeedVectorScale_Cuda()
748 y_impl->h_array = NULL; in CeedVectorAXPY_Cuda()
749 } else if (y_impl->h_array) { in CeedVectorAXPY_Cuda()
751 CeedCallBackend(CeedHostAXPY_Cuda(y_impl->h_array, alpha, x_impl->h_array, length)); in CeedVectorAXPY_Cuda()
785 if (y_impl->h_array) { in CeedVectorAXPBY_Cuda()
787 CeedCallBackend(CeedHostAXPBY_Cuda(y_impl->h_array, alpha, beta, x_impl->h_array, length)); in CeedVectorAXPBY_Cuda()
817 if (!w_impl->d_array && !w_impl->h_array) { in CeedVectorPointwiseMult_Cuda()
825 if (w_impl->h_array) { in CeedVectorPointwiseMult_Cuda()
828 …CeedCallBackend(CeedHostPointwiseMult_Cuda(w_impl->h_array, x_impl->h_array, y_impl->h_array, leng… in CeedVectorPointwiseMult_Cuda()