Lines Matching refs:length
42 CeedSize length; in CeedVectorSyncH2D_Cuda() local
50 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSyncH2D_Cuda()
51 bytes = length * sizeof(CeedScalar); in CeedVectorSyncH2D_Cuda()
68 CeedSize length; in CeedVectorSyncD2H_Cuda() local
80 CeedSize length; in CeedVectorSyncD2H_Cuda() local
82 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSyncD2H_Cuda()
83 CeedCallBackend(CeedCalloc(length, &impl->h_array_owned)); in CeedVectorSyncD2H_Cuda()
87 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSyncD2H_Cuda()
88 size_t bytes = length * sizeof(CeedScalar); in CeedVectorSyncD2H_Cuda()
176 CeedSize length; in CeedVectorSetArrayHost_Cuda() local
180 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSetArrayHost_Cuda()
182 …CeedCallBackend(CeedSetHostCeedScalarArray(array, copy_mode, length, (const CeedScalar **)&impl->h… in CeedVectorSetArrayHost_Cuda()
191 CeedSize length; in CeedVectorSetArrayDevice_Cuda() local
197 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSetArrayDevice_Cuda()
199 …CeedCallBackend(CeedSetDeviceCeedScalarArray_Cuda(ceed, array, copy_mode, length, (const CeedScala… in CeedVectorSetArrayDevice_Cuda()
240 CeedSize length; in CeedVectorCopyStrided_Cuda() local
249 length = length_vec < length_copy ? length_vec : length_copy; in CeedVectorCopyStrided_Cuda()
251 if (stop == -1) stop = length; 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()
298 int CeedDeviceSetValue_Cuda(CeedScalar *d_array, CeedSize length, CeedScalar val);
304 CeedSize length; in CeedVectorSetValue_Cuda() local
308 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSetValue_Cuda()
325 …CeedCallCuda(CeedVectorReturnCeed(vec), cudaMemset(impl->d_array, 0, length * sizeof(CeedScalar))); in CeedVectorSetValue_Cuda()
327 CeedCallBackend(CeedDeviceSetValue_Cuda(impl->d_array, length, val)); in CeedVectorSetValue_Cuda()
331 CeedCallBackend(CeedHostSetValue_Cuda(impl->h_array, length, val)); in CeedVectorSetValue_Cuda()
354 CeedSize length; in CeedVectorSetValueStrided_Cuda() local
358 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorSetValueStrided_Cuda()
360 if (stop == -1) stop = length; in CeedVectorSetValueStrided_Cuda()
479 CeedSize length; in CeedVectorNorm_Cuda() local
489 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorNorm_Cuda()
496 num_calls = length / INT_MAX; in CeedVectorNorm_Cuda()
497 if (length % INT_MAX > 0) num_calls += 1; in CeedVectorNorm_Cuda()
507 … CeedCallCublas(ceed, cublasSasum_64(handle, (int64_t)length, (float *)d_array, 1, (float *)norm)); in CeedVectorNorm_Cuda()
514 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Cuda()
523 …CeedCallCublas(ceed, cublasDasum_64(handle, (int64_t)length, (double *)d_array, 1, (double *)norm)… in CeedVectorNorm_Cuda()
530 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Cuda()
543 … CeedCallCublas(ceed, cublasSnrm2_64(handle, (int64_t)length, (float *)d_array, 1, (float *)norm)); in CeedVectorNorm_Cuda()
550 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Cuda()
560 …CeedCallCublas(ceed, cublasDnrm2_64(handle, (int64_t)length, (double *)d_array, 1, (double *)norm)… in CeedVectorNorm_Cuda()
567 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Cuda()
584 CeedCallCublas(ceed, cublasIsamax_64(handle, (int64_t)length, (float *)d_array, 1, &index)); in CeedVectorNorm_Cuda()
594 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Cuda()
608 CeedCallCublas(ceed, cublasIdamax_64(handle, (int64_t)length, (double *)d_array, 1, &index)); in CeedVectorNorm_Cuda()
618 CeedSize remaining_length = length - (CeedSize)(i)*INT_MAX; in CeedVectorNorm_Cuda()
639 static int CeedHostReciprocal_Cuda(CeedScalar *h_array, CeedSize length) { in CeedHostReciprocal_Cuda() argument
640 for (CeedSize i = 0; i < length; i++) { in CeedHostReciprocal_Cuda()
649 int CeedDeviceReciprocal_Cuda(CeedScalar *d_array, CeedSize length);
655 CeedSize length; in CeedVectorReciprocal_Cuda() local
659 CeedCallBackend(CeedVectorGetLength(vec, &length)); in CeedVectorReciprocal_Cuda()
661 if (impl->d_array) CeedCallBackend(CeedDeviceReciprocal_Cuda(impl->d_array, length)); in CeedVectorReciprocal_Cuda()
662 if (impl->h_array) CeedCallBackend(CeedHostReciprocal_Cuda(impl->h_array, length)); in CeedVectorReciprocal_Cuda()
669 static int CeedHostScale_Cuda(CeedScalar *x_array, CeedScalar alpha, CeedSize length) { in CeedHostScale_Cuda() argument
670 for (CeedSize i = 0; i < length; i++) x_array[i] *= alpha; in CeedHostScale_Cuda()
677 int CeedDeviceScale_Cuda(CeedScalar *x_array, CeedScalar alpha, CeedSize length);
683 CeedSize length; in CeedVectorScale_Cuda() local
687 CeedCallBackend(CeedVectorGetLength(x, &length)); in CeedVectorScale_Cuda()
695 …CeedCallCublas(CeedVectorReturnCeed(x), cublasSscal_64(handle, (int64_t)length, &alpha, impl->d_ar… in CeedVectorScale_Cuda()
697 …CeedCallCublas(CeedVectorReturnCeed(x), cublasDscal_64(handle, (int64_t)length, &alpha, impl->d_ar… in CeedVectorScale_Cuda()
700 CeedCallBackend(CeedDeviceScale_Cuda(impl->d_array, alpha, length)); in CeedVectorScale_Cuda()
704 CeedCallBackend(CeedHostScale_Cuda(impl->h_array, alpha, length)); in CeedVectorScale_Cuda()
713 …nt CeedHostAXPY_Cuda(CeedScalar *y_array, CeedScalar alpha, CeedScalar *x_array, CeedSize length) { in CeedHostAXPY_Cuda() argument
714 for (CeedSize i = 0; i < length; i++) y_array[i] += alpha * x_array[i]; in CeedHostAXPY_Cuda()
721 int CeedDeviceAXPY_Cuda(CeedScalar *y_array, CeedScalar alpha, CeedScalar *x_array, CeedSize length…
727 CeedSize length; in CeedVectorAXPY_Cuda() local
732 CeedCallBackend(CeedVectorGetLength(y, &length)); in CeedVectorAXPY_Cuda()
741 …CeedCallCublas(CeedVectorReturnCeed(y), cublasSaxpy_64(handle, (int64_t)length, &alpha, x_impl->d_… in CeedVectorAXPY_Cuda()
743 …CeedCallCublas(CeedVectorReturnCeed(y), cublasDaxpy_64(handle, (int64_t)length, &alpha, x_impl->d_… in CeedVectorAXPY_Cuda()
746 CeedCallBackend(CeedDeviceAXPY_Cuda(y_impl->d_array, alpha, x_impl->d_array, length)); in CeedVectorAXPY_Cuda()
751 CeedCallBackend(CeedHostAXPY_Cuda(y_impl->h_array, alpha, x_impl->h_array, length)); in CeedVectorAXPY_Cuda()
760 …uda(CeedScalar *y_array, CeedScalar alpha, CeedScalar beta, CeedScalar *x_array, CeedSize length) { in CeedHostAXPBY_Cuda() argument
761 for (CeedSize i = 0; i < length; i++) y_array[i] = alpha * x_array[i] + beta * y_array[i]; in CeedHostAXPBY_Cuda()
768 …Cuda(CeedScalar *y_array, CeedScalar alpha, CeedScalar beta, CeedScalar *x_array, CeedSize length);
774 CeedSize length; in CeedVectorAXPBY_Cuda() local
779 CeedCallBackend(CeedVectorGetLength(y, &length)); in CeedVectorAXPBY_Cuda()
783 CeedCallBackend(CeedDeviceAXPBY_Cuda(y_impl->d_array, alpha, beta, x_impl->d_array, length)); in CeedVectorAXPBY_Cuda()
787 CeedCallBackend(CeedHostAXPBY_Cuda(y_impl->h_array, alpha, beta, x_impl->h_array, length)); in CeedVectorAXPBY_Cuda()
795 …ointwiseMult_Cuda(CeedScalar *w_array, CeedScalar *x_array, CeedScalar *y_array, CeedSize length) { in CeedHostPointwiseMult_Cuda() argument
796 for (CeedSize i = 0; i < length; i++) w_array[i] = x_array[i] * y_array[i]; in CeedHostPointwiseMult_Cuda()
803 …PointwiseMult_Cuda(CeedScalar *w_array, CeedScalar *x_array, CeedScalar *y_array, CeedSize length);
809 CeedSize length; in CeedVectorPointwiseMult_Cuda() local
815 CeedCallBackend(CeedVectorGetLength(w, &length)); in CeedVectorPointwiseMult_Cuda()
823 …llBackend(CeedDevicePointwiseMult_Cuda(w_impl->d_array, x_impl->d_array, y_impl->d_array, length)); in CeedVectorPointwiseMult_Cuda()
828 …CallBackend(CeedHostPointwiseMult_Cuda(w_impl->h_array, x_impl->h_array, y_impl->h_array, length)); in CeedVectorPointwiseMult_Cuda()