Lines Matching refs:length
42 CeedSize length; in CeedVectorSyncH2D_Hip() local
50 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSyncH2D_Hip()
51 bytes = length * sizeof(CeedScalar); in CeedVectorSyncH2D_Hip()
68 CeedSize length; in CeedVectorSyncD2H_Hip() local
81 CeedSize length; in CeedVectorSyncD2H_Hip() local
83 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSyncD2H_Hip()
84 CeedCallBackend(CeedCalloc(length, &impl->h_array_owned)); in CeedVectorSyncD2H_Hip()
88 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSyncD2H_Hip()
89 bytes = length * sizeof(CeedScalar); in CeedVectorSyncD2H_Hip()
188 CeedSize length; in CeedVectorSetArrayHost_Hip() local
192 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSetArrayHost_Hip()
194 …CeedCallBackend(CeedSetHostCeedScalarArray(array, copy_mode, length, (const CeedScalar **)&impl->h… in CeedVectorSetArrayHost_Hip()
203 CeedSize length; in CeedVectorSetArrayDevice_Hip() local
209 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSetArrayDevice_Hip()
211 …CeedCallBackend(CeedSetDeviceCeedScalarArray_Hip(ceed, array, copy_mode, length, (const CeedScalar… in CeedVectorSetArrayDevice_Hip()
221 CeedSize length; in CeedVectorSetArrayUnifiedHostToDevice_Hip() local
227 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSetArrayUnifiedHostToDevice_Hip()
236 …ay_owned) CeedCallHip(ceed, hipMalloc((void **)&impl->d_array_owned, sizeof(CeedScalar) * length)); in CeedVectorSetArrayUnifiedHostToDevice_Hip()
240 …if (array) CeedCallHip(ceed, hipMemcpy(impl->d_array, array, sizeof(CeedScalar) * length, hipMemcp… in CeedVectorSetArrayUnifiedHostToDevice_Hip()
293 CeedSize length; in CeedVectorCopyStrided_Hip() local
302 length = length_vec < length_copy ? length_vec : length_copy; in CeedVectorCopyStrided_Hip()
304 if (stop == -1) stop = length; in CeedVectorCopyStrided_Hip()
345 static int CeedHostSetValue_Hip(CeedScalar *h_array, CeedSize length, CeedScalar val) { in CeedHostSetValue_Hip() argument
346 for (CeedSize i = 0; i < length; i++) h_array[i] = val; in CeedHostSetValue_Hip()
353 int CeedDeviceSetValue_Hip(CeedScalar *d_array, CeedSize length, CeedScalar val);
359 CeedSize length; in CeedVectorSetValue_Hip() local
365 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSetValue_Hip()
382 … CeedCallHip(CeedVectorReturnCeed(vec), hipMemset(impl->d_array, 0, length * sizeof(CeedScalar))); in CeedVectorSetValue_Hip()
384 CeedCallBackend(CeedDeviceSetValue_Hip(impl->d_array, length, val)); in CeedVectorSetValue_Hip()
388 CeedCallBackend(CeedHostSetValue_Hip(impl->h_array, length, val)); in CeedVectorSetValue_Hip()
411 CeedSize length; in CeedVectorSetValueStrided_Hip() local
415 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSetValueStrided_Hip()
417 if (stop == -1) stop = length; in CeedVectorSetValueStrided_Hip()
555 CeedSize length; in CeedVectorNorm_Hip() local
568 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorNorm_Hip()
575 num_calls = length / INT_MAX; in CeedVectorNorm_Hip()
576 if (length % INT_MAX > 0) num_calls += 1; in CeedVectorNorm_Hip()
586 …CeedCallHipblas(ceed, hipblasSasum_64(handle, (int64_t)length, (float *)d_array, 1, (float *)norm)… in CeedVectorNorm_Hip()
594 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Hip()
604 …CeedCallHipblas(ceed, hipblasDasum_64(handle, (int64_t)length, (double *)d_array, 1, (double *)nor… in CeedVectorNorm_Hip()
612 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Hip()
626 …CeedCallHipblas(ceed, hipblasSnrm2_64(handle, (int64_t)length, (float *)d_array, 1, (float *)norm)… in CeedVectorNorm_Hip()
634 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Hip()
645 …CeedCallHipblas(ceed, hipblasDnrm2_64(handle, (int64_t)length, (double *)d_array, 1, (double *)nor… in CeedVectorNorm_Hip()
653 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Hip()
671 CeedCallHipblas(ceed, hipblasIsamax_64(handle, (int64_t)length, (float *)d_array, 1, &index)); in CeedVectorNorm_Hip()
682 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Hip()
702 … CeedCallHipblas(ceed, hipblasIdamax_64(handle, (int64_t)length, (double *)d_array, 1, &index)); in CeedVectorNorm_Hip()
718 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Hip()
745 static int CeedHostReciprocal_Hip(CeedScalar *h_array, CeedSize length) { in CeedHostReciprocal_Hip() argument
746 for (CeedSize i = 0; i < length; i++) { in CeedHostReciprocal_Hip()
755 int CeedDeviceReciprocal_Hip(CeedScalar *d_array, CeedSize length);
761 CeedSize length; in CeedVectorReciprocal_Hip() local
765 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorReciprocal_Hip()
767 if (impl->d_array) CeedCallBackend(CeedDeviceReciprocal_Hip(impl->d_array, length)); in CeedVectorReciprocal_Hip()
768 if (impl->h_array) CeedCallBackend(CeedHostReciprocal_Hip(impl->h_array, length)); in CeedVectorReciprocal_Hip()
775 static int CeedHostScale_Hip(CeedScalar *x_array, CeedScalar alpha, CeedSize length) { in CeedHostScale_Hip() argument
776 for (CeedSize i = 0; i < length; i++) x_array[i] *= alpha; in CeedHostScale_Hip()
783 int CeedDeviceScale_Hip(CeedScalar *x_array, CeedScalar alpha, CeedSize length);
789 CeedSize length; in CeedVectorScale_Hip() local
793 CeedCallBackend(CeedVectorGetLength(x, &length)); in CeedVectorScale_Hip()
803 …CeedCallHipblas(CeedVectorReturnCeed(x), hipblasSscal_64(handle, (int64_t)length, &alpha, impl->d_… in CeedVectorScale_Hip()
805 …CeedCallHipblas(CeedVectorReturnCeed(x), hipblasDscal_64(handle, (int64_t)length, &alpha, impl->d_… in CeedVectorScale_Hip()
809 CeedCallBackend(CeedDeviceScale_Hip(impl->d_array, alpha, length)); in CeedVectorScale_Hip()
814 CeedCallBackend(CeedHostScale_Hip(impl->h_array, alpha, length)); in CeedVectorScale_Hip()
823 …int CeedHostAXPY_Hip(CeedScalar *y_array, CeedScalar alpha, CeedScalar *x_array, CeedSize length) { in CeedHostAXPY_Hip() argument
824 for (CeedSize i = 0; i < length; i++) y_array[i] += alpha * x_array[i]; in CeedHostAXPY_Hip()
831 int CeedDeviceAXPY_Hip(CeedScalar *y_array, CeedScalar alpha, CeedScalar *x_array, CeedSize length);
837 CeedSize length; in CeedVectorAXPY_Hip() local
842 CeedCallBackend(CeedVectorGetLength(y, &length)); in CeedVectorAXPY_Hip()
853 …CeedCallHipblas(CeedVectorReturnCeed(y), hipblasSaxpy_64(handle, (int64_t)length, &alpha, x_impl->… in CeedVectorAXPY_Hip()
855 …CeedCallHipblas(CeedVectorReturnCeed(y), hipblasDaxpy_64(handle, (int64_t)length, &alpha, x_impl->… in CeedVectorAXPY_Hip()
859 CeedCallBackend(CeedDeviceAXPY_Hip(y_impl->d_array, alpha, x_impl->d_array, length)); in CeedVectorAXPY_Hip()
864 CeedCallBackend(CeedHostAXPY_Hip(y_impl->h_array, alpha, x_impl->h_array, length)); in CeedVectorAXPY_Hip()
873 …Hip(CeedScalar *y_array, CeedScalar alpha, CeedScalar beta, CeedScalar *x_array, CeedSize length) { in CeedHostAXPBY_Hip() argument
874 for (CeedSize i = 0; i < length; i++) y_array[i] = alpha * x_array[i] + beta * y_array[i]; in CeedHostAXPBY_Hip()
881 …_Hip(CeedScalar *y_array, CeedScalar alpha, CeedScalar beta, CeedScalar *x_array, CeedSize length);
887 CeedSize length; in CeedVectorAXPBY_Hip() local
892 CeedCallBackend(CeedVectorGetLength(y, &length)); in CeedVectorAXPBY_Hip()
896 CeedCallBackend(CeedDeviceAXPBY_Hip(y_impl->d_array, alpha, beta, x_impl->d_array, length)); in CeedVectorAXPBY_Hip()
900 CeedCallBackend(CeedHostAXPBY_Hip(y_impl->h_array, alpha, beta, x_impl->h_array, length)); in CeedVectorAXPBY_Hip()
908 …PointwiseMult_Hip(CeedScalar *w_array, CeedScalar *x_array, CeedScalar *y_array, CeedSize length) { in CeedHostPointwiseMult_Hip() argument
909 for (CeedSize i = 0; i < length; i++) w_array[i] = x_array[i] * y_array[i]; in CeedHostPointwiseMult_Hip()
916 …ePointwiseMult_Hip(CeedScalar *w_array, CeedScalar *x_array, CeedScalar *y_array, CeedSize length);
922 CeedSize length; in CeedVectorPointwiseMult_Hip() local
928 CeedCallBackend(CeedVectorGetLength(w, &length)); in CeedVectorPointwiseMult_Hip()
937 …allBackend(CeedDevicePointwiseMult_Hip(w_impl->d_array, x_impl->d_array, y_impl->d_array, length)); in CeedVectorPointwiseMult_Hip()
942 …dCallBackend(CeedHostPointwiseMult_Hip(w_impl->h_array, x_impl->h_array, y_impl->h_array, length)); in CeedVectorPointwiseMult_Hip()