Mercurial > hgrepos > Python2 > PyMuPDF
diff mupdf-source/thirdparty/tesseract/src/arch/dotproductneon.cpp @ 2:b50eed0cc0ef upstream
ADD: MuPDF v1.26.7: the MuPDF source as downloaded by a default build of PyMuPDF 1.26.4.
The directory name has changed: no version number in the expanded directory now.
| author | Franz Glasner <fzglas.hg@dom66.de> |
|---|---|
| date | Mon, 15 Sep 2025 11:43:07 +0200 |
| parents | |
| children |
line wrap: on
line diff
--- /dev/null Thu Jan 01 00:00:00 1970 +0000 +++ b/mupdf-source/thirdparty/tesseract/src/arch/dotproductneon.cpp Mon Sep 15 11:43:07 2025 +0200 @@ -0,0 +1,71 @@ +/////////////////////////////////////////////////////////////////////// +// File: dotproductneon.cpp +// Description: Dot product function for ARM NEON. +// Author: Stefan Weil +// +// Licensed under the Apache License, Version 2.0 (the "License"); +// you may not use this file except in compliance with the License. +// You may obtain a copy of the License at +// http://www.apache.org/licenses/LICENSE-2.0 +// Unless required by applicable law or agreed to in writing, software +// distributed under the License is distributed on an "AS IS" BASIS, +// WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied. +// See the License for the specific language governing permissions and +// limitations under the License. +/////////////////////////////////////////////////////////////////////// + +#if defined(__ARM_NEON) + +#include <arm_neon.h> +#include "dotproduct.h" + +namespace tesseract { + +// Documentation: +// https://developer.arm.com/architectures/instruction-sets/intrinsics/ + +#if defined(FAST_FLOAT) && defined(__ARM_ARCH_ISA_A64) + +float DotProductNEON(const float *u, const float *v, int n) { + float32x4_t result0123 = vdupq_n_f32(0.0f); + float32x4_t result4567 = vdupq_n_f32(0.0f); + while (n > 7) { + // Calculate 8 dot products per iteration. + float32x4_t u0 = vld1q_f32(u); + float32x4_t v0 = vld1q_f32(v); + float32x4_t u4 = vld1q_f32(u + 4); + float32x4_t v4 = vld1q_f32(v + 4); + result0123 = vfmaq_f32(result0123, u0, v0); + result4567 = vfmaq_f32(result4567, u4, v4); + u += 8; + v += 8; + n -= 8; + } + float total = vaddvq_f32(result0123); + total += vaddvq_f32(result4567); + while (n > 0) { + total += *u++ * *v++; + n--; + } + return total; +} + +#else + +// Computes and returns the dot product of the two n-vectors u and v. +TFloat DotProductNEON(const TFloat *u, const TFloat *v, int n) { + TFloat total = 0; +#if defined(OPENMP_SIMD) || defined(_OPENMP) +#pragma omp simd reduction(+:total) +#endif + for (int k = 0; k < n; k++) { + total += u[k] * v[k]; + } + return total; +} + +#endif + +} // namespace tesseract + +#endif /* __ARM_NEON */
