Rename vunop and vbinop functions
- Normalize names with other microkernel-related functions and files. Only operator-related functions have "op" in the name.
- vunop -> vunary
- vbinop -> vbinary
PiperOrigin-RevId: 281864878
diff --git a/src/f32-sigmoid/neon-frac-p9-p10-nr1recps-x16.c b/src/f32-sigmoid/neon-frac-p9-p10-nr1recps-x16.c
index 994f7af..b66f073 100644
--- a/src/f32-sigmoid/neon-frac-p9-p10-nr1recps-x16.c
+++ b/src/f32-sigmoid/neon-frac-p9-p10-nr1recps-x16.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
void xnn_f32_sigmoid_ukernel__neon_frac_p9_p10_nr1recps_x16(
diff --git a/src/f32-sigmoid/neon-frac-p9-p10-nr1recps.c.in b/src/f32-sigmoid/neon-frac-p9-p10-nr1recps.c.in
index 012b8eb..434f86e 100644
--- a/src/f32-sigmoid/neon-frac-p9-p10-nr1recps.c.in
+++ b/src/f32-sigmoid/neon-frac-p9-p10-nr1recps.c.in
@@ -11,7 +11,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
void xnn_f32_sigmoid_ukernel__neon_frac_p9_p10_nr1recps_x${BATCH_TILE}(
diff --git a/src/f32-sigmoid/neonfma-p5-nr2fma-x16.c b/src/f32-sigmoid/neonfma-p5-nr2fma-x16.c
index 5555154..0c8ac1b 100644
--- a/src/f32-sigmoid/neonfma-p5-nr2fma-x16.c
+++ b/src/f32-sigmoid/neonfma-p5-nr2fma-x16.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
void xnn_f32_sigmoid_ukernel__neonfma_p5_nr2fma_x16(
diff --git a/src/f32-sigmoid/neonfma-p5-nr2fma.c.in b/src/f32-sigmoid/neonfma-p5-nr2fma.c.in
index c11b062..fe952bf 100644
--- a/src/f32-sigmoid/neonfma-p5-nr2fma.c.in
+++ b/src/f32-sigmoid/neonfma-p5-nr2fma.c.in
@@ -11,7 +11,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
void xnn_f32_sigmoid_ukernel__neonfma_p5_nr2fma_x${BATCH_TILE}(
diff --git a/src/f32-sigmoid/sse-p5-div.c.in b/src/f32-sigmoid/sse-p5-div.c.in
index e3c1a00..4ae3897 100644
--- a/src/f32-sigmoid/sse-p5-div.c.in
+++ b/src/f32-sigmoid/sse-p5-div.c.in
@@ -14,7 +14,7 @@
#include <emmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
void xnn_f32_sigmoid_ukernel__${"sse41" if BLEND else "sse2"}_p5_div_x${BATCH_TILE}(
diff --git a/src/f32-sigmoid/sse2-p5-div-x16.c b/src/f32-sigmoid/sse2-p5-div-x16.c
index 7dbc685..5e232cf 100644
--- a/src/f32-sigmoid/sse2-p5-div-x16.c
+++ b/src/f32-sigmoid/sse2-p5-div-x16.c
@@ -12,7 +12,7 @@
#include <emmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
void xnn_f32_sigmoid_ukernel__sse2_p5_div_x16(
diff --git a/src/f32-sigmoid/sse2-p5-div-x8.c b/src/f32-sigmoid/sse2-p5-div-x8.c
index c869639..bf9bf94 100644
--- a/src/f32-sigmoid/sse2-p5-div-x8.c
+++ b/src/f32-sigmoid/sse2-p5-div-x8.c
@@ -12,7 +12,7 @@
#include <emmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
void xnn_f32_sigmoid_ukernel__sse2_p5_div_x8(
diff --git a/src/f32-sigmoid/sse2-p5-div.c.in b/src/f32-sigmoid/sse2-p5-div.c.in
new file mode 100644
index 0000000..ab02615
--- /dev/null
+++ b/src/f32-sigmoid/sse2-p5-div.c.in
@@ -0,0 +1,286 @@
+// Copyright 2019 Google LLC
+//
+// This source code is licensed under the BSD-style license found in the
+// LICENSE file in the root directory of this source tree.
+
+$assert BATCH_TILE % 4 == 0
+$assert BATCH_TILE >= 4
+$ABC = "0123456789ABCDEFGHIJKLMN"
+#include <assert.h>
+
+#include <emmintrin.h>
+
+#include <xnnpack/common.h>
+#include <xnnpack/vunary.h>
+
+
+void xnn_f32_sigmoid_ukernel__sse2_p5_div_x${BATCH_TILE}(
+ size_t n,
+ const float* x,
+ float* y,
+ const void* params)
+{
+ assert(n % sizeof(float) == 0);
+
+ const __m128 vmagic_bias = _mm_set1_ps(0x1.8000FEp23f);
+ // The smallest x for which sigmoidf(x) is normalized.
+ // This number is also the smallest x for which expf(x) is normalized.
+ const __m128 vdenorm_cutoff = _mm_set1_ps(-0x1.5D589Ep+6f);
+ // The largest x for which sigmoidf(x) is not equal 1.0.
+ const __m128 vone_cutoff = _mm_set1_ps(0x1.154244p+4f);
+ const __m128 vlog2e = _mm_set1_ps(0x1.715476p+0f);
+ // Last 8 bits are zeroes
+ const __m128 vminus_ln2_hi = _mm_set1_ps(-0x1.62E400p-1f);
+ const __m128 vminus_ln2_lo = _mm_set1_ps(-0x1.7F7D1Cp-20f);
+ const __m128 vone = _mm_set1_ps(1.0f);
+ const __m128 vsign_mask = _mm_set1_ps(-0.0f);
+
+ const __m128 vc1 = _mm_set1_ps(0x1.FFFFF6p-1f);
+ const __m128 vc2 = _mm_set1_ps(0x1.FFFDC6p-2f);
+ const __m128 vc3 = _mm_set1_ps(0x1.555A80p-3f);
+ const __m128 vc4 = _mm_set1_ps(0x1.573A1Ap-5f);
+ const __m128 vc5 = _mm_set1_ps(0x1.0F9F9Cp-7f);
+
+ for (; n >= ${BATCH_TILE} * sizeof(float); n -= ${BATCH_TILE} * sizeof(float)) {
+ const __m128 vx${ABC[0:4]} = _mm_loadu_ps(x);
+ $for N in range(4, BATCH_TILE, 4):
+ const __m128 vx${ABC[N:N+4]} = _mm_loadu_ps(x + ${N});
+
+ // General structure of the algorithm:
+ // / exp(x) / (1 + exp(x)) if x <= 0
+ // f[x] :=
+ // \ 1 - f[-x] if x >= 0
+ //
+ // First we compute f[z] := exp(z) / (1 + exp(z)) where z = -abs(x),
+ // then replace result with 1 - f[z] if x >= 0.
+ $for N in range(0, BATCH_TILE, 4):
+ const __m128 vz${ABC[N:N+4]} = _mm_or_ps(vx${ABC[N:N+4]}, vsign_mask);
+
+ // Compute reduced argument n := round(z / log(2)).
+ // We do it by adding a large number (magic bias) to the product z * (1/log(2)), which cause rounding of the result
+ // to an integer, then subtracing the large number back. The trick with adding large number is valid only within
+ // certain bounds (|x| <= 2**22), but thats ok, because inputs x outside of [-87.336544, 17.328678] (i.e. z outsize
+ // [0, 87.336544]) underflow or saturate sigmoidf(x) anyway. We fixup the result for such inputs at the very end of
+ // the algorithm.
+ $for N in range(0, BATCH_TILE, 4):
+ __m128 vn${ABC[N:N+4]} = _mm_add_ps(_mm_mul_ps(vz${ABC[N:N+4]}, vlog2e), vmagic_bias);
+
+ // Create a floating-point number s (scale) such that s == 2**n for inputs which don't cause underflow, i.e.
+ // -87.33642 <= z <= 0.0, and -126 <= n <= 0 accordingly.
+ $for N in range(0, BATCH_TILE, 4):
+ const __m128 vs${ABC[N:N+4]} = _mm_castsi128_ps(_mm_slli_epi32(_mm_castps_si128(vn${ABC[N:N+4]}), 23));
+
+ // Subtract the large number back to get final n := round(z / log(2)).
+ $for N in range(0, BATCH_TILE, 4):
+ vn${ABC[N:N+4]} = _mm_sub_ps(vn${ABC[N:N+4]}, vmagic_bias);
+
+ // Compute reduced argument t := z - n * log(2).
+ // Use Cody-Waite range reduction method (note two constants to represent log(2)) to improve accuracy.
+ $for N in range(0, BATCH_TILE, 4):
+ __m128 vt${ABC[N:N+4]} = _mm_add_ps(_mm_mul_ps(vn${ABC[N:N+4]}, vminus_ln2_hi), vz${ABC[N:N+4]});
+
+ $for N in range(0, BATCH_TILE, 4):
+ vt${ABC[N:N+4]} = _mm_add_ps(_mm_mul_ps(vn${ABC[N:N+4]}, vminus_ln2_lo), vt${ABC[N:N+4]});
+
+ // Compute degree-5 polynomial approxiatmion for exp(t) on [-log(2)/2, log(2)/2].
+ $for N in range(0, BATCH_TILE, 4):
+ __m128 vp${ABC[N:N+4]} = _mm_add_ps(_mm_mul_ps(vc5, vt${ABC[N:N+4]}), vc4);
+
+ $for N in range(0, BATCH_TILE, 4):
+ vp${ABC[N:N+4]} = _mm_add_ps(_mm_mul_ps(vp${ABC[N:N+4]}, vt${ABC[N:N+4]}), vc3);
+
+ $for N in range(0, BATCH_TILE, 4):
+ vp${ABC[N:N+4]} = _mm_add_ps(_mm_mul_ps(vp${ABC[N:N+4]}, vt${ABC[N:N+4]}), vc2);
+
+ $for N in range(0, BATCH_TILE, 4):
+ vp${ABC[N:N+4]} = _mm_add_ps(_mm_mul_ps(vp${ABC[N:N+4]}, vt${ABC[N:N+4]}), vc1);
+
+ // Reconstruct the exp(z) value:
+ // e = s * (1 + t * (c1 + t * (c2 + t * (c3 + t * (c4 + t * c5)))))
+ // = s + (t * s) * (c1 + t * (c2 + t * (c3 + t * (c4 + t * c5))))
+ // = s + (t * s) * p
+ $for N in range(0, BATCH_TILE, 4):
+ vt${ABC[N:N+4]} = _mm_mul_ps(vt${ABC[N:N+4]}, vs${ABC[N:N+4]});
+
+ $for N in range(0, BATCH_TILE, 4):
+ __m128 ve${ABC[N:N+4]} = _mm_add_ps(_mm_mul_ps(vt${ABC[N:N+4]}, vp${ABC[N:N+4]}), vs${ABC[N:N+4]});
+
+ // Denominator of the sigmoid fraction: 1.0 + exp(z)
+ $for N in range(0, BATCH_TILE, 4):
+ __m128 vd${ABC[N:N+4]} = _mm_add_ps(ve${ABC[N:N+4]}, vone);
+
+ // Reconstruct sigmoid(-z) = exp(z) / (1.0 + exp(z))
+ $for N in range(0, BATCH_TILE, 4):
+ __m128 vf${ABC[N:N+4]} = _mm_div_ps(ve${ABC[N:N+4]}, vd${ABC[N:N+4]});
+
+ // Reconstruct sigmoid(x) = x < 0 ? sigmoid(z) : 1.0 - sigmoid(z)
+ $for N in range(0, BATCH_TILE, 4):
+ __m128 vm${ABC[N:N+4]} = _mm_castsi128_ps(_mm_cmpgt_epi32(_mm_setzero_si128(), _mm_castps_si128(vx${ABC[N:N+4]})));
+
+ $for N in range(0, BATCH_TILE, 4):
+ vf${ABC[N:N+4]} = _mm_or_ps(_mm_and_ps(vf${ABC[N:N+4]}, vm${ABC[N:N+4]}), _mm_andnot_ps(vm${ABC[N:N+4]}, _mm_sub_ps(vone, vf${ABC[N:N+4]})));
+
+ // For inputs above 1.0 cutoff, replace output with 1.0.
+ // Note that for NaN inputs, comparison result is false, and outputs are left unchanged.
+ $for N in range(0, BATCH_TILE, 4):
+ vm${ABC[N:N+4]} = _mm_cmpgt_ps(vx${ABC[N:N+4]}, vone_cutoff);
+
+ $for N in range(0, BATCH_TILE, 4):
+ vf${ABC[N:N+4]} = _mm_or_ps(_mm_and_ps(vone, vm${ABC[N:N+4]}), _mm_andnot_ps(vm${ABC[N:N+4]}, vf${ABC[N:N+4]}));
+
+ // For inputs below denormal cutoff, replace output with +0.0f.
+ // Note that for NaN inputs, comparison result is false, and outputs are left unchanged.
+ $for N in range(0, BATCH_TILE, 4):
+ vf${ABC[N:N+4]} = _mm_andnot_ps(_mm_cmplt_ps(vx${ABC[N:N+4]}, vdenorm_cutoff), vf${ABC[N:N+4]});
+
+ _mm_storeu_ps(y, vf${ABC[0:4]});
+ $for N in range(4, BATCH_TILE, 4):
+ _mm_storeu_ps(y + ${N}, vf${ABC[N:N+4]});
+
+ x += ${BATCH_TILE};
+ y += ${BATCH_TILE};
+ }
+ $if BATCH_TILE > 4:
+ for (; n >= 4 * sizeof(float); n -= 4 * sizeof(float)) {
+ const __m128 vx0123 = _mm_loadu_ps(x);
+
+ // General structure of the algorithm:
+ // / exp(x) / (1 + exp(x)) if x <= 0
+ // f[x] :=
+ // \ 1 - f[-x] if x >= 0
+ //
+ // First we compute f[z] := exp(z) / (1 + exp(z)) where z = -abs(x),
+ // then replace result with 1 - f[z] if x >= 0.
+ const __m128 vz0123 = _mm_or_ps(vx0123, vsign_mask);
+
+ // Compute reduced argument n := round(z / log(2)).
+ // We do it by adding a large number (magic bias) to the product z * (1/log(2)), which cause rounding of the result
+ // to an integer, then subtracing the large number back. The trick with adding large number is valid only within
+ // certain bounds (|x| <= 2**22), but thats ok, because inputs x outside of [-87.336544, 17.328678] (i.e. z outsize
+ // [0, 87.336544]) underflow or saturate sigmoidf(x) anyway. We fixup the result for such inputs at the very end of
+ // the algorithm.
+ __m128 vn0123 = _mm_add_ps(_mm_mul_ps(vz0123, vlog2e), vmagic_bias);
+
+ // Create a floating-point number s (scale) such that s == 2**n for inputs which don't cause underflow, i.e.
+ // -87.33642 <= z <= 0.0, and -126 <= n <= 0 accordingly.
+ const __m128 vs0123 = _mm_castsi128_ps(_mm_slli_epi32(_mm_castps_si128(vn0123), 23));
+
+ // Subtract the large number back to get final n := round(z / log(2)).
+ vn0123 = _mm_sub_ps(vn0123, vmagic_bias);
+
+ // Compute reduced argument t := z - n * log(2).
+ // Use Cody-Waite range reduction method (note two constants to represent log(2)) to improve accuracy.
+ __m128 vt0123 = _mm_add_ps(_mm_mul_ps(vn0123, vminus_ln2_hi), vz0123);
+ vt0123 = _mm_add_ps(_mm_mul_ps(vn0123, vminus_ln2_lo), vt0123);
+
+ // Compute degree-5 polynomial approxiatmion for exp(t) on [-log(2)/2, log(2)/2].
+ __m128 vp0123 = _mm_add_ps(_mm_mul_ps(vc5, vt0123), vc4);
+ vp0123 = _mm_add_ps(_mm_mul_ps(vp0123, vt0123), vc3);
+ vp0123 = _mm_add_ps(_mm_mul_ps(vp0123, vt0123), vc2);
+ vp0123 = _mm_add_ps(_mm_mul_ps(vp0123, vt0123), vc1);
+
+ // Reconstruct the exp(z) value:
+ // e = s * (1 + t * (c1 + t * (c2 + t * (c3 + t * (c4 + t * c5)))))
+ // = s + (t * s) * (c1 + t * (c2 + t * (c3 + t * (c4 + t * c5))))
+ // = s + (t * s) * p
+ vt0123 = _mm_mul_ps(vt0123, vs0123);
+ __m128 ve0123 = _mm_add_ps(_mm_mul_ps(vt0123, vp0123), vs0123);
+
+ // Denominator of the sigmoid fraction: 1.0 + exp(z)
+ __m128 vd0123 = _mm_add_ps(ve0123, vone);
+
+ // Reconstruct sigmoid(-z) = exp(z) / (1.0 + exp(z))
+ __m128 vf0123 = _mm_div_ps(ve0123, vd0123);
+
+ // Reconstruct sigmoid(x) = x < 0 ? sigmoid(z) : 1.0 - sigmoid(z)
+ __m128 vm0123 = _mm_castsi128_ps(_mm_cmpgt_epi32(_mm_setzero_si128(), _mm_castps_si128(vx0123)));
+ vf0123 = _mm_or_ps(_mm_and_ps(vf0123, vm0123), _mm_andnot_ps(vm0123, _mm_sub_ps(vone, vf0123)));
+
+ // For inputs above 1.0 cutoff, replace output with 1.0.
+ // Note that for NaN inputs, comparison result is false, and outputs are left unchanged.
+ vm0123 = _mm_cmpgt_ps(vx0123, vone_cutoff);
+ vf0123 = _mm_or_ps(_mm_and_ps(vone, vm0123), _mm_andnot_ps(vm0123, vf0123));
+
+ // For inputs below denormal cutoff, replace output with +0.0f.
+ // Note that for NaN inputs, comparison result is false, and outputs are left unchanged.
+ vf0123 = _mm_andnot_ps(_mm_cmplt_ps(vx0123, vdenorm_cutoff), vf0123);
+
+ _mm_storeu_ps(y, vf0123);
+
+ x += 4;
+ y += 4;
+ }
+ if XNN_UNLIKELY(n != 0) {
+ const __m128 vx0123 = _mm_loadu_ps(x);
+
+ // General structure of the algorithm:
+ // / exp(x) / (1 + exp(x)) if x <= 0
+ // f[x] :=
+ // \ 1 - f[-x] if x >= 0
+ //
+ // First we compute f[z] := exp(z) / (1 + exp(z)) where z = -abs(x),
+ // then replace result with 1 - f[z] if x >= 0.
+ const __m128 vz0123 = _mm_or_ps(vx0123, vsign_mask);
+
+ // Compute reduced argument n := round(z / log(2)).
+ // We do it by adding a large number (magic bias) to the product z * (1/log(2)), which cause rounding of the result
+ // to an integer, then subtracing the large number back. The trick with adding large number is valid only within
+ // certain bounds (|x| <= 2**22), but thats ok, because inputs x outside of [-87.336544, 17.328678] (i.e. z outsize
+ // [0, 87.336544]) underflow or saturate sigmoidf(x) anyway. We fixup the result for such inputs at the very end of
+ // the algorithm.
+ __m128 vn0123 = _mm_add_ps(_mm_mul_ps(vz0123, vlog2e), vmagic_bias);
+
+ // Create a floating-point number s (scale) such that s == 2**n for inputs which don't cause underflow, i.e.
+ // -87.33642 <= z <= 0.0, and -126 <= n <= 0 accordingly.
+ const __m128 vs0123 = _mm_castsi128_ps(_mm_slli_epi32(_mm_castps_si128(vn0123), 23));
+
+ // Subtract the large number back to get final n := round(z / log(2)).
+ vn0123 = _mm_sub_ps(vn0123, vmagic_bias);
+
+ // Compute reduced argument t := z - n * log(2).
+ // Use Cody-Waite range reduction method (note two constants to represent log(2)) to improve accuracy.
+ __m128 vt0123 = _mm_add_ps(_mm_mul_ps(vn0123, vminus_ln2_hi), vz0123);
+ vt0123 = _mm_add_ps(_mm_mul_ps(vn0123, vminus_ln2_lo), vt0123);
+
+ // Compute degree-5 polynomial approxiatmion for exp(t) on [-log(2)/2, log(2)/2].
+ __m128 vp0123 = _mm_add_ps(_mm_mul_ps(vc5, vt0123), vc4);
+ vp0123 = _mm_add_ps(_mm_mul_ps(vp0123, vt0123), vc3);
+ vp0123 = _mm_add_ps(_mm_mul_ps(vp0123, vt0123), vc2);
+ vp0123 = _mm_add_ps(_mm_mul_ps(vp0123, vt0123), vc1);
+
+ // Reconstruct the exp(z) value:
+ // e = s * (1 + t * (c1 + t * (c2 + t * (c3 + t * (c4 + t * c5)))))
+ // = s + (t * s) * (c1 + t * (c2 + t * (c3 + t * (c4 + t * c5))))
+ // = s + (t * s) * p
+ vt0123 = _mm_mul_ps(vt0123, vs0123);
+ __m128 ve0123 = _mm_add_ps(_mm_mul_ps(vt0123, vp0123), vs0123);
+
+ // Denominator of the sigmoid fraction: 1.0 + exp(z)
+ __m128 vd0123 = _mm_add_ps(ve0123, vone);
+
+ // Reconstruct sigmoid(-z) = exp(z) / (1.0 + exp(z))
+ __m128 vf0123 = _mm_div_ps(ve0123, vd0123);
+
+ // Reconstruct sigmoid(x) = x < 0 ? sigmoid(z) : 1.0 - sigmoid(z)
+ __m128 vm0123 = _mm_castsi128_ps(_mm_cmpgt_epi32(_mm_setzero_si128(), _mm_castps_si128(vx0123)));
+ vf0123 = _mm_or_ps(_mm_and_ps(vf0123, vm0123), _mm_andnot_ps(vm0123, _mm_sub_ps(vone, vf0123)));
+
+ // For inputs above 1.0 cutoff, replace output with 1.0.
+ // Note that for NaN inputs, comparison result is false, and outputs are left unchanged.
+ vm0123 = _mm_cmpgt_ps(vx0123, vone_cutoff);
+ vf0123 = _mm_or_ps(_mm_and_ps(vone, vm0123), _mm_andnot_ps(vm0123, vf0123));
+
+ // For inputs below denormal cutoff, replace output with +0.0f.
+ // Note that for NaN inputs, comparison result is false, and outputs are left unchanged.
+ vf0123 = _mm_andnot_ps(_mm_cmplt_ps(vx0123, vdenorm_cutoff), vf0123);
+
+ if (n & (2 * sizeof(float))) {
+ _mm_storel_pi((__m64*) y, vf0123);
+ vf0123 = _mm_movehl_ps(vf0123, vf0123);
+ y += 2;
+ }
+ if (n & (1 * sizeof(float))) {
+ _mm_store_ss(y, vf0123);
+ }
+ }
+}
diff --git a/src/f32-sigmoid/sse41-p5-div-x16.c b/src/f32-sigmoid/sse41-p5-div-x16.c
index 092eef0..cf95fec 100644
--- a/src/f32-sigmoid/sse41-p5-div-x16.c
+++ b/src/f32-sigmoid/sse41-p5-div-x16.c
@@ -12,7 +12,7 @@
#include <smmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
void xnn_f32_sigmoid_ukernel__sse41_p5_div_x16(
diff --git a/src/f32-sigmoid/sse41-p5-div-x8.c b/src/f32-sigmoid/sse41-p5-div-x8.c
index 69957a4..a2c16a5 100644
--- a/src/f32-sigmoid/sse41-p5-div-x8.c
+++ b/src/f32-sigmoid/sse41-p5-div-x8.c
@@ -12,7 +12,7 @@
#include <smmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
void xnn_f32_sigmoid_ukernel__sse41_p5_div_x8(
diff --git a/src/f32-binop/vadd-neon-x4.c b/src/f32-vbinary/vadd-neon-x4.c
similarity index 98%
rename from src/f32-binop/vadd-neon-x4.c
rename to src/f32-vbinary/vadd-neon-x4.c
index 97566f4..9e74662 100644
--- a/src/f32-binop/vadd-neon-x4.c
+++ b/src/f32-vbinary/vadd-neon-x4.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vadd_ukernel__neon_x4(
diff --git a/src/f32-binop/vadd-neon-x8.c b/src/f32-vbinary/vadd-neon-x8.c
similarity index 98%
rename from src/f32-binop/vadd-neon-x8.c
rename to src/f32-vbinary/vadd-neon-x8.c
index b71b5e4..fffdcb7 100644
--- a/src/f32-binop/vadd-neon-x8.c
+++ b/src/f32-vbinary/vadd-neon-x8.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vadd_ukernel__neon_x8(
diff --git a/src/f32-binop/vadd-psimd-x4.c b/src/f32-vbinary/vadd-psimd-x4.c
similarity index 98%
rename from src/f32-binop/vadd-psimd-x4.c
rename to src/f32-vbinary/vadd-psimd-x4.c
index 145917c..8c98c88 100644
--- a/src/f32-binop/vadd-psimd-x4.c
+++ b/src/f32-vbinary/vadd-psimd-x4.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vadd_ukernel__psimd_x4(
diff --git a/src/f32-binop/vadd-psimd-x8.c b/src/f32-vbinary/vadd-psimd-x8.c
similarity index 98%
rename from src/f32-binop/vadd-psimd-x8.c
rename to src/f32-vbinary/vadd-psimd-x8.c
index e52b614..41d8e90 100644
--- a/src/f32-binop/vadd-psimd-x8.c
+++ b/src/f32-vbinary/vadd-psimd-x8.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vadd_ukernel__psimd_x8(
diff --git a/src/f32-binop/vadd-scalar-x1.c b/src/f32-vbinary/vadd-scalar-x1.c
similarity index 96%
rename from src/f32-binop/vadd-scalar-x1.c
rename to src/f32-vbinary/vadd-scalar-x1.c
index f71539f..11e9031 100644
--- a/src/f32-binop/vadd-scalar-x1.c
+++ b/src/f32-vbinary/vadd-scalar-x1.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vadd_ukernel__scalar_x1(
diff --git a/src/f32-binop/vadd-scalar-x2.c b/src/f32-vbinary/vadd-scalar-x2.c
similarity index 97%
rename from src/f32-binop/vadd-scalar-x2.c
rename to src/f32-vbinary/vadd-scalar-x2.c
index d4931fd..25e21f3 100644
--- a/src/f32-binop/vadd-scalar-x2.c
+++ b/src/f32-vbinary/vadd-scalar-x2.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vadd_ukernel__scalar_x2(
diff --git a/src/f32-binop/vadd-scalar-x4.c b/src/f32-vbinary/vadd-scalar-x4.c
similarity index 98%
rename from src/f32-binop/vadd-scalar-x4.c
rename to src/f32-vbinary/vadd-scalar-x4.c
index a285245..761bbbe 100644
--- a/src/f32-binop/vadd-scalar-x4.c
+++ b/src/f32-vbinary/vadd-scalar-x4.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vadd_ukernel__scalar_x4(
diff --git a/src/f32-binop/vadd-sse-x4.c b/src/f32-vbinary/vadd-sse-x4.c
similarity index 98%
rename from src/f32-binop/vadd-sse-x4.c
rename to src/f32-vbinary/vadd-sse-x4.c
index 7b09071..a73e9e6 100644
--- a/src/f32-binop/vadd-sse-x4.c
+++ b/src/f32-vbinary/vadd-sse-x4.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vadd_ukernel__sse_x4(
diff --git a/src/f32-binop/vadd-sse-x8.c b/src/f32-vbinary/vadd-sse-x8.c
similarity index 98%
rename from src/f32-binop/vadd-sse-x8.c
rename to src/f32-vbinary/vadd-sse-x8.c
index 92d5219..0e58308 100644
--- a/src/f32-binop/vadd-sse-x8.c
+++ b/src/f32-vbinary/vadd-sse-x8.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vadd_ukernel__sse_x8(
diff --git a/src/f32-binop/vaddc-neon-x4.c b/src/f32-vbinary/vaddc-neon-x4.c
similarity index 98%
rename from src/f32-binop/vaddc-neon-x4.c
rename to src/f32-vbinary/vaddc-neon-x4.c
index 0fc102d..8c911de 100644
--- a/src/f32-binop/vaddc-neon-x4.c
+++ b/src/f32-vbinary/vaddc-neon-x4.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vaddc_ukernel__neon_x4(
diff --git a/src/f32-binop/vaddc-neon-x8.c b/src/f32-vbinary/vaddc-neon-x8.c
similarity index 98%
rename from src/f32-binop/vaddc-neon-x8.c
rename to src/f32-vbinary/vaddc-neon-x8.c
index 0ba792f..907a7e5 100644
--- a/src/f32-binop/vaddc-neon-x8.c
+++ b/src/f32-vbinary/vaddc-neon-x8.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vaddc_ukernel__neon_x8(
diff --git a/src/f32-binop/vaddc-psimd-x4.c b/src/f32-vbinary/vaddc-psimd-x4.c
similarity index 98%
rename from src/f32-binop/vaddc-psimd-x4.c
rename to src/f32-vbinary/vaddc-psimd-x4.c
index 8a7ca57..ac68b36 100644
--- a/src/f32-binop/vaddc-psimd-x4.c
+++ b/src/f32-vbinary/vaddc-psimd-x4.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vaddc_ukernel__psimd_x4(
diff --git a/src/f32-binop/vaddc-psimd-x8.c b/src/f32-vbinary/vaddc-psimd-x8.c
similarity index 98%
rename from src/f32-binop/vaddc-psimd-x8.c
rename to src/f32-vbinary/vaddc-psimd-x8.c
index dd70d25..afa7ad1 100644
--- a/src/f32-binop/vaddc-psimd-x8.c
+++ b/src/f32-vbinary/vaddc-psimd-x8.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vaddc_ukernel__psimd_x8(
diff --git a/src/f32-binop/vaddc-scalar-x1.c b/src/f32-vbinary/vaddc-scalar-x1.c
similarity index 96%
rename from src/f32-binop/vaddc-scalar-x1.c
rename to src/f32-vbinary/vaddc-scalar-x1.c
index 2ae3ffe..d591020 100644
--- a/src/f32-binop/vaddc-scalar-x1.c
+++ b/src/f32-vbinary/vaddc-scalar-x1.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vaddc_ukernel__scalar_x1(
diff --git a/src/f32-binop/vaddc-scalar-x2.c b/src/f32-vbinary/vaddc-scalar-x2.c
similarity index 97%
rename from src/f32-binop/vaddc-scalar-x2.c
rename to src/f32-vbinary/vaddc-scalar-x2.c
index 677b3bf..a41445e 100644
--- a/src/f32-binop/vaddc-scalar-x2.c
+++ b/src/f32-vbinary/vaddc-scalar-x2.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vaddc_ukernel__scalar_x2(
diff --git a/src/f32-binop/vaddc-scalar-x4.c b/src/f32-vbinary/vaddc-scalar-x4.c
similarity index 97%
rename from src/f32-binop/vaddc-scalar-x4.c
rename to src/f32-vbinary/vaddc-scalar-x4.c
index 21caa29..92792d9 100644
--- a/src/f32-binop/vaddc-scalar-x4.c
+++ b/src/f32-vbinary/vaddc-scalar-x4.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vaddc_ukernel__scalar_x4(
diff --git a/src/f32-binop/vaddc-sse-x4.c b/src/f32-vbinary/vaddc-sse-x4.c
similarity index 97%
rename from src/f32-binop/vaddc-sse-x4.c
rename to src/f32-vbinary/vaddc-sse-x4.c
index e18007d..4442a01 100644
--- a/src/f32-binop/vaddc-sse-x4.c
+++ b/src/f32-vbinary/vaddc-sse-x4.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vaddc_ukernel__sse_x4(
diff --git a/src/f32-binop/vaddc-sse-x8.c b/src/f32-vbinary/vaddc-sse-x8.c
similarity index 98%
rename from src/f32-binop/vaddc-sse-x8.c
rename to src/f32-vbinary/vaddc-sse-x8.c
index 6fc13f6..6580953 100644
--- a/src/f32-binop/vaddc-sse-x8.c
+++ b/src/f32-vbinary/vaddc-sse-x8.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vaddc_ukernel__sse_x8(
diff --git a/src/f32-binop/vmul-neon-x4.c b/src/f32-vbinary/vmul-neon-x4.c
similarity index 98%
rename from src/f32-binop/vmul-neon-x4.c
rename to src/f32-vbinary/vmul-neon-x4.c
index 873051d..93df938 100644
--- a/src/f32-binop/vmul-neon-x4.c
+++ b/src/f32-vbinary/vmul-neon-x4.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmul_ukernel__neon_x4(
diff --git a/src/f32-binop/vmul-neon-x8.c b/src/f32-vbinary/vmul-neon-x8.c
similarity index 98%
rename from src/f32-binop/vmul-neon-x8.c
rename to src/f32-vbinary/vmul-neon-x8.c
index d543a63..7cdb655 100644
--- a/src/f32-binop/vmul-neon-x8.c
+++ b/src/f32-vbinary/vmul-neon-x8.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmul_ukernel__neon_x8(
diff --git a/src/f32-binop/vmul-psimd-x4.c b/src/f32-vbinary/vmul-psimd-x4.c
similarity index 98%
rename from src/f32-binop/vmul-psimd-x4.c
rename to src/f32-vbinary/vmul-psimd-x4.c
index df9ee0e..7802a34 100644
--- a/src/f32-binop/vmul-psimd-x4.c
+++ b/src/f32-vbinary/vmul-psimd-x4.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmul_ukernel__psimd_x4(
diff --git a/src/f32-binop/vmul-psimd-x8.c b/src/f32-vbinary/vmul-psimd-x8.c
similarity index 98%
rename from src/f32-binop/vmul-psimd-x8.c
rename to src/f32-vbinary/vmul-psimd-x8.c
index 1149da4..c51e94e 100644
--- a/src/f32-binop/vmul-psimd-x8.c
+++ b/src/f32-vbinary/vmul-psimd-x8.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmul_ukernel__psimd_x8(
diff --git a/src/f32-binop/vmul-scalar-x1.c b/src/f32-vbinary/vmul-scalar-x1.c
similarity index 96%
rename from src/f32-binop/vmul-scalar-x1.c
rename to src/f32-vbinary/vmul-scalar-x1.c
index 33567c5..2f47570 100644
--- a/src/f32-binop/vmul-scalar-x1.c
+++ b/src/f32-vbinary/vmul-scalar-x1.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmul_ukernel__scalar_x1(
diff --git a/src/f32-binop/vmul-scalar-x2.c b/src/f32-vbinary/vmul-scalar-x2.c
similarity index 97%
rename from src/f32-binop/vmul-scalar-x2.c
rename to src/f32-vbinary/vmul-scalar-x2.c
index cf46b7d..317be4f 100644
--- a/src/f32-binop/vmul-scalar-x2.c
+++ b/src/f32-vbinary/vmul-scalar-x2.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmul_ukernel__scalar_x2(
diff --git a/src/f32-binop/vmul-scalar-x4.c b/src/f32-vbinary/vmul-scalar-x4.c
similarity index 98%
rename from src/f32-binop/vmul-scalar-x4.c
rename to src/f32-vbinary/vmul-scalar-x4.c
index bab1c56..a840d27 100644
--- a/src/f32-binop/vmul-scalar-x4.c
+++ b/src/f32-vbinary/vmul-scalar-x4.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmul_ukernel__scalar_x4(
diff --git a/src/f32-binop/vmul-sse-x4.c b/src/f32-vbinary/vmul-sse-x4.c
similarity index 98%
rename from src/f32-binop/vmul-sse-x4.c
rename to src/f32-vbinary/vmul-sse-x4.c
index ab1f096..a100481 100644
--- a/src/f32-binop/vmul-sse-x4.c
+++ b/src/f32-vbinary/vmul-sse-x4.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmul_ukernel__sse_x4(
diff --git a/src/f32-binop/vmul-sse-x8.c b/src/f32-vbinary/vmul-sse-x8.c
similarity index 98%
rename from src/f32-binop/vmul-sse-x8.c
rename to src/f32-vbinary/vmul-sse-x8.c
index f4e8909..b9849f6 100644
--- a/src/f32-binop/vmul-sse-x8.c
+++ b/src/f32-vbinary/vmul-sse-x8.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmul_ukernel__sse_x8(
diff --git a/src/f32-binop/vmulc-neon-x4.c b/src/f32-vbinary/vmulc-neon-x4.c
similarity index 98%
rename from src/f32-binop/vmulc-neon-x4.c
rename to src/f32-vbinary/vmulc-neon-x4.c
index 1926c92..8b4b8d5 100644
--- a/src/f32-binop/vmulc-neon-x4.c
+++ b/src/f32-vbinary/vmulc-neon-x4.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmulc_ukernel__neon_x4(
diff --git a/src/f32-binop/vmulc-neon-x8.c b/src/f32-vbinary/vmulc-neon-x8.c
similarity index 98%
rename from src/f32-binop/vmulc-neon-x8.c
rename to src/f32-vbinary/vmulc-neon-x8.c
index 971fbf8..8b362e5 100644
--- a/src/f32-binop/vmulc-neon-x8.c
+++ b/src/f32-vbinary/vmulc-neon-x8.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmulc_ukernel__neon_x8(
diff --git a/src/f32-binop/vmulc-psimd-x4.c b/src/f32-vbinary/vmulc-psimd-x4.c
similarity index 98%
rename from src/f32-binop/vmulc-psimd-x4.c
rename to src/f32-vbinary/vmulc-psimd-x4.c
index 552fc9d..cbb9ae6 100644
--- a/src/f32-binop/vmulc-psimd-x4.c
+++ b/src/f32-vbinary/vmulc-psimd-x4.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmulc_ukernel__psimd_x4(
diff --git a/src/f32-binop/vmulc-psimd-x8.c b/src/f32-vbinary/vmulc-psimd-x8.c
similarity index 98%
rename from src/f32-binop/vmulc-psimd-x8.c
rename to src/f32-vbinary/vmulc-psimd-x8.c
index 2a55630..4a5fbe4 100644
--- a/src/f32-binop/vmulc-psimd-x8.c
+++ b/src/f32-vbinary/vmulc-psimd-x8.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmulc_ukernel__psimd_x8(
diff --git a/src/f32-binop/vmulc-scalar-x1.c b/src/f32-vbinary/vmulc-scalar-x1.c
similarity index 96%
rename from src/f32-binop/vmulc-scalar-x1.c
rename to src/f32-vbinary/vmulc-scalar-x1.c
index 33e1b1e..b0a485a 100644
--- a/src/f32-binop/vmulc-scalar-x1.c
+++ b/src/f32-vbinary/vmulc-scalar-x1.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmulc_ukernel__scalar_x1(
diff --git a/src/f32-binop/vmulc-scalar-x2.c b/src/f32-vbinary/vmulc-scalar-x2.c
similarity index 97%
rename from src/f32-binop/vmulc-scalar-x2.c
rename to src/f32-vbinary/vmulc-scalar-x2.c
index 6c55f10..7d58a74 100644
--- a/src/f32-binop/vmulc-scalar-x2.c
+++ b/src/f32-vbinary/vmulc-scalar-x2.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmulc_ukernel__scalar_x2(
diff --git a/src/f32-binop/vmulc-scalar-x4.c b/src/f32-vbinary/vmulc-scalar-x4.c
similarity index 97%
rename from src/f32-binop/vmulc-scalar-x4.c
rename to src/f32-vbinary/vmulc-scalar-x4.c
index 82917a5..c8888fc 100644
--- a/src/f32-binop/vmulc-scalar-x4.c
+++ b/src/f32-vbinary/vmulc-scalar-x4.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmulc_ukernel__scalar_x4(
diff --git a/src/f32-binop/vmulc-sse-x4.c b/src/f32-vbinary/vmulc-sse-x4.c
similarity index 97%
rename from src/f32-binop/vmulc-sse-x4.c
rename to src/f32-vbinary/vmulc-sse-x4.c
index 6793c85..8dafee9 100644
--- a/src/f32-binop/vmulc-sse-x4.c
+++ b/src/f32-vbinary/vmulc-sse-x4.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmulc_ukernel__sse_x4(
diff --git a/src/f32-binop/vmulc-sse-x8.c b/src/f32-vbinary/vmulc-sse-x8.c
similarity index 98%
rename from src/f32-binop/vmulc-sse-x8.c
rename to src/f32-vbinary/vmulc-sse-x8.c
index fa57654..0f7f892 100644
--- a/src/f32-binop/vmulc-sse-x8.c
+++ b/src/f32-vbinary/vmulc-sse-x8.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vmulc_ukernel__sse_x8(
diff --git a/src/f32-binop/vop-neon.c.in b/src/f32-vbinary/vop-neon.c.in
similarity index 98%
rename from src/f32-binop/vop-neon.c.in
rename to src/f32-vbinary/vop-neon.c.in
index d635849..7018fc6 100644
--- a/src/f32-binop/vop-neon.c.in
+++ b/src/f32-vbinary/vop-neon.c.in
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
$VOPQ_F32 = {
diff --git a/src/f32-binop/vop-psimd.c.in b/src/f32-vbinary/vop-psimd.c.in
similarity index 98%
rename from src/f32-binop/vop-psimd.c.in
rename to src/f32-vbinary/vop-psimd.c.in
index ece6eca..0ba0dcf 100644
--- a/src/f32-binop/vop-psimd.c.in
+++ b/src/f32-vbinary/vop-psimd.c.in
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
$PSIMD_OP_F32 = {
diff --git a/src/f32-binop/vop-scalar.c.in b/src/f32-vbinary/vop-scalar.c.in
similarity index 98%
rename from src/f32-binop/vop-scalar.c.in
rename to src/f32-vbinary/vop-scalar.c.in
index ab6cfba..633218a 100644
--- a/src/f32-binop/vop-scalar.c.in
+++ b/src/f32-vbinary/vop-scalar.c.in
@@ -10,7 +10,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
$OP_FUNC = {
diff --git a/src/f32-binop/vop-sse.c.in b/src/f32-vbinary/vop-sse.c.in
similarity index 98%
rename from src/f32-binop/vop-sse.c.in
rename to src/f32-vbinary/vop-sse.c.in
index 45a4247..d19b794 100644
--- a/src/f32-binop/vop-sse.c.in
+++ b/src/f32-vbinary/vop-sse.c.in
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
$_MM_OP_PS = {
diff --git a/src/f32-binop/vopc-neon.c.in b/src/f32-vbinary/vopc-neon.c.in
similarity index 98%
rename from src/f32-binop/vopc-neon.c.in
rename to src/f32-vbinary/vopc-neon.c.in
index 2916336..dbf214f 100644
--- a/src/f32-binop/vopc-neon.c.in
+++ b/src/f32-vbinary/vopc-neon.c.in
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
$VOPQ_F32 = {
diff --git a/src/f32-binop/vopc-psimd.c.in b/src/f32-vbinary/vopc-psimd.c.in
similarity index 98%
rename from src/f32-binop/vopc-psimd.c.in
rename to src/f32-vbinary/vopc-psimd.c.in
index ae12d21..6402f59 100644
--- a/src/f32-binop/vopc-psimd.c.in
+++ b/src/f32-vbinary/vopc-psimd.c.in
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
$PSIMD_OP_F32 = {
diff --git a/src/f32-binop/vopc-scalar.c.in b/src/f32-vbinary/vopc-scalar.c.in
similarity index 98%
rename from src/f32-binop/vopc-scalar.c.in
rename to src/f32-vbinary/vopc-scalar.c.in
index 410d7e5..88fb010 100644
--- a/src/f32-binop/vopc-scalar.c.in
+++ b/src/f32-vbinary/vopc-scalar.c.in
@@ -10,7 +10,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
$OP_FUNC = {
diff --git a/src/f32-binop/vopc-sse.c.in b/src/f32-vbinary/vopc-sse.c.in
similarity index 98%
rename from src/f32-binop/vopc-sse.c.in
rename to src/f32-vbinary/vopc-sse.c.in
index 44dd95e..aae6bd1 100644
--- a/src/f32-binop/vopc-sse.c.in
+++ b/src/f32-vbinary/vopc-sse.c.in
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
$_MM_OP_PS = {
diff --git a/src/f32-binop/vrsubc-neon-x4.c b/src/f32-vbinary/vrsubc-neon-x4.c
similarity index 98%
rename from src/f32-binop/vrsubc-neon-x4.c
rename to src/f32-vbinary/vrsubc-neon-x4.c
index 49cbfac..b185e54 100644
--- a/src/f32-binop/vrsubc-neon-x4.c
+++ b/src/f32-vbinary/vrsubc-neon-x4.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vrsubc_ukernel__neon_x4(
diff --git a/src/f32-binop/vrsubc-neon-x8.c b/src/f32-vbinary/vrsubc-neon-x8.c
similarity index 98%
rename from src/f32-binop/vrsubc-neon-x8.c
rename to src/f32-vbinary/vrsubc-neon-x8.c
index 5242e23..fcaf1d4 100644
--- a/src/f32-binop/vrsubc-neon-x8.c
+++ b/src/f32-vbinary/vrsubc-neon-x8.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vrsubc_ukernel__neon_x8(
diff --git a/src/f32-binop/vrsubc-psimd-x4.c b/src/f32-vbinary/vrsubc-psimd-x4.c
similarity index 98%
rename from src/f32-binop/vrsubc-psimd-x4.c
rename to src/f32-vbinary/vrsubc-psimd-x4.c
index 92c7bcb..80cf600 100644
--- a/src/f32-binop/vrsubc-psimd-x4.c
+++ b/src/f32-vbinary/vrsubc-psimd-x4.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vrsubc_ukernel__psimd_x4(
diff --git a/src/f32-binop/vrsubc-psimd-x8.c b/src/f32-vbinary/vrsubc-psimd-x8.c
similarity index 98%
rename from src/f32-binop/vrsubc-psimd-x8.c
rename to src/f32-vbinary/vrsubc-psimd-x8.c
index 98f1645..0518f5f 100644
--- a/src/f32-binop/vrsubc-psimd-x8.c
+++ b/src/f32-vbinary/vrsubc-psimd-x8.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vrsubc_ukernel__psimd_x8(
diff --git a/src/f32-binop/vrsubc-scalar-x1.c b/src/f32-vbinary/vrsubc-scalar-x1.c
similarity index 96%
rename from src/f32-binop/vrsubc-scalar-x1.c
rename to src/f32-vbinary/vrsubc-scalar-x1.c
index defd37b..338a439 100644
--- a/src/f32-binop/vrsubc-scalar-x1.c
+++ b/src/f32-vbinary/vrsubc-scalar-x1.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vrsubc_ukernel__scalar_x1(
diff --git a/src/f32-binop/vrsubc-scalar-x2.c b/src/f32-vbinary/vrsubc-scalar-x2.c
similarity index 97%
rename from src/f32-binop/vrsubc-scalar-x2.c
rename to src/f32-vbinary/vrsubc-scalar-x2.c
index 63a9d88..2d10e46 100644
--- a/src/f32-binop/vrsubc-scalar-x2.c
+++ b/src/f32-vbinary/vrsubc-scalar-x2.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vrsubc_ukernel__scalar_x2(
diff --git a/src/f32-binop/vrsubc-scalar-x4.c b/src/f32-vbinary/vrsubc-scalar-x4.c
similarity index 97%
rename from src/f32-binop/vrsubc-scalar-x4.c
rename to src/f32-vbinary/vrsubc-scalar-x4.c
index 7ac3b94..03c5923 100644
--- a/src/f32-binop/vrsubc-scalar-x4.c
+++ b/src/f32-vbinary/vrsubc-scalar-x4.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vrsubc_ukernel__scalar_x4(
diff --git a/src/f32-binop/vrsubc-sse-x4.c b/src/f32-vbinary/vrsubc-sse-x4.c
similarity index 97%
rename from src/f32-binop/vrsubc-sse-x4.c
rename to src/f32-vbinary/vrsubc-sse-x4.c
index 910174e..0cf727e 100644
--- a/src/f32-binop/vrsubc-sse-x4.c
+++ b/src/f32-vbinary/vrsubc-sse-x4.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vrsubc_ukernel__sse_x4(
diff --git a/src/f32-binop/vrsubc-sse-x8.c b/src/f32-vbinary/vrsubc-sse-x8.c
similarity index 98%
rename from src/f32-binop/vrsubc-sse-x8.c
rename to src/f32-vbinary/vrsubc-sse-x8.c
index 84a4bde..48137f4 100644
--- a/src/f32-binop/vrsubc-sse-x8.c
+++ b/src/f32-vbinary/vrsubc-sse-x8.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vrsubc_ukernel__sse_x8(
diff --git a/src/f32-binop/vsub-neon-x4.c b/src/f32-vbinary/vsub-neon-x4.c
similarity index 98%
rename from src/f32-binop/vsub-neon-x4.c
rename to src/f32-vbinary/vsub-neon-x4.c
index ec345dd..859aa62 100644
--- a/src/f32-binop/vsub-neon-x4.c
+++ b/src/f32-vbinary/vsub-neon-x4.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsub_ukernel__neon_x4(
diff --git a/src/f32-binop/vsub-neon-x8.c b/src/f32-vbinary/vsub-neon-x8.c
similarity index 98%
rename from src/f32-binop/vsub-neon-x8.c
rename to src/f32-vbinary/vsub-neon-x8.c
index cfbfe06..0bd9fa2 100644
--- a/src/f32-binop/vsub-neon-x8.c
+++ b/src/f32-vbinary/vsub-neon-x8.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsub_ukernel__neon_x8(
diff --git a/src/f32-binop/vsub-psimd-x4.c b/src/f32-vbinary/vsub-psimd-x4.c
similarity index 98%
rename from src/f32-binop/vsub-psimd-x4.c
rename to src/f32-vbinary/vsub-psimd-x4.c
index c1cbd74..de35ab2 100644
--- a/src/f32-binop/vsub-psimd-x4.c
+++ b/src/f32-vbinary/vsub-psimd-x4.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsub_ukernel__psimd_x4(
diff --git a/src/f32-binop/vsub-psimd-x8.c b/src/f32-vbinary/vsub-psimd-x8.c
similarity index 98%
rename from src/f32-binop/vsub-psimd-x8.c
rename to src/f32-vbinary/vsub-psimd-x8.c
index 6160cc5..a0bd614 100644
--- a/src/f32-binop/vsub-psimd-x8.c
+++ b/src/f32-vbinary/vsub-psimd-x8.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsub_ukernel__psimd_x8(
diff --git a/src/f32-binop/vsub-scalar-x1.c b/src/f32-vbinary/vsub-scalar-x1.c
similarity index 96%
rename from src/f32-binop/vsub-scalar-x1.c
rename to src/f32-vbinary/vsub-scalar-x1.c
index 47591a2..6f88531 100644
--- a/src/f32-binop/vsub-scalar-x1.c
+++ b/src/f32-vbinary/vsub-scalar-x1.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsub_ukernel__scalar_x1(
diff --git a/src/f32-binop/vsub-scalar-x2.c b/src/f32-vbinary/vsub-scalar-x2.c
similarity index 97%
rename from src/f32-binop/vsub-scalar-x2.c
rename to src/f32-vbinary/vsub-scalar-x2.c
index 106c79f..b9948ff 100644
--- a/src/f32-binop/vsub-scalar-x2.c
+++ b/src/f32-vbinary/vsub-scalar-x2.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsub_ukernel__scalar_x2(
diff --git a/src/f32-binop/vsub-scalar-x4.c b/src/f32-vbinary/vsub-scalar-x4.c
similarity index 98%
rename from src/f32-binop/vsub-scalar-x4.c
rename to src/f32-vbinary/vsub-scalar-x4.c
index 5e8bab3..dca0c77 100644
--- a/src/f32-binop/vsub-scalar-x4.c
+++ b/src/f32-vbinary/vsub-scalar-x4.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsub_ukernel__scalar_x4(
diff --git a/src/f32-binop/vsub-sse-x4.c b/src/f32-vbinary/vsub-sse-x4.c
similarity index 98%
rename from src/f32-binop/vsub-sse-x4.c
rename to src/f32-vbinary/vsub-sse-x4.c
index 832c40a..d8c23be 100644
--- a/src/f32-binop/vsub-sse-x4.c
+++ b/src/f32-vbinary/vsub-sse-x4.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsub_ukernel__sse_x4(
diff --git a/src/f32-binop/vsub-sse-x8.c b/src/f32-vbinary/vsub-sse-x8.c
similarity index 98%
rename from src/f32-binop/vsub-sse-x8.c
rename to src/f32-vbinary/vsub-sse-x8.c
index e0e0d52..0c157a3 100644
--- a/src/f32-binop/vsub-sse-x8.c
+++ b/src/f32-vbinary/vsub-sse-x8.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsub_ukernel__sse_x8(
diff --git a/src/f32-binop/vsubc-neon-x4.c b/src/f32-vbinary/vsubc-neon-x4.c
similarity index 98%
rename from src/f32-binop/vsubc-neon-x4.c
rename to src/f32-vbinary/vsubc-neon-x4.c
index 690802d..eab5204 100644
--- a/src/f32-binop/vsubc-neon-x4.c
+++ b/src/f32-vbinary/vsubc-neon-x4.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsubc_ukernel__neon_x4(
diff --git a/src/f32-binop/vsubc-neon-x8.c b/src/f32-vbinary/vsubc-neon-x8.c
similarity index 98%
rename from src/f32-binop/vsubc-neon-x8.c
rename to src/f32-vbinary/vsubc-neon-x8.c
index ad7e72f..18cd847 100644
--- a/src/f32-binop/vsubc-neon-x8.c
+++ b/src/f32-vbinary/vsubc-neon-x8.c
@@ -12,7 +12,7 @@
#include <arm_neon.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsubc_ukernel__neon_x8(
diff --git a/src/f32-binop/vsubc-psimd-x4.c b/src/f32-vbinary/vsubc-psimd-x4.c
similarity index 98%
rename from src/f32-binop/vsubc-psimd-x4.c
rename to src/f32-vbinary/vsubc-psimd-x4.c
index 911e375..54b4ece 100644
--- a/src/f32-binop/vsubc-psimd-x4.c
+++ b/src/f32-vbinary/vsubc-psimd-x4.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsubc_ukernel__psimd_x4(
diff --git a/src/f32-binop/vsubc-psimd-x8.c b/src/f32-vbinary/vsubc-psimd-x8.c
similarity index 98%
rename from src/f32-binop/vsubc-psimd-x8.c
rename to src/f32-vbinary/vsubc-psimd-x8.c
index 0c08465..f393a93 100644
--- a/src/f32-binop/vsubc-psimd-x8.c
+++ b/src/f32-vbinary/vsubc-psimd-x8.c
@@ -12,7 +12,7 @@
#include <psimd.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsubc_ukernel__psimd_x8(
diff --git a/src/f32-binop/vsubc-scalar-x1.c b/src/f32-vbinary/vsubc-scalar-x1.c
similarity index 96%
rename from src/f32-binop/vsubc-scalar-x1.c
rename to src/f32-vbinary/vsubc-scalar-x1.c
index c252c94..7a346af 100644
--- a/src/f32-binop/vsubc-scalar-x1.c
+++ b/src/f32-vbinary/vsubc-scalar-x1.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsubc_ukernel__scalar_x1(
diff --git a/src/f32-binop/vsubc-scalar-x2.c b/src/f32-vbinary/vsubc-scalar-x2.c
similarity index 97%
rename from src/f32-binop/vsubc-scalar-x2.c
rename to src/f32-vbinary/vsubc-scalar-x2.c
index 57bdd74..3b40715 100644
--- a/src/f32-binop/vsubc-scalar-x2.c
+++ b/src/f32-vbinary/vsubc-scalar-x2.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsubc_ukernel__scalar_x2(
diff --git a/src/f32-binop/vsubc-scalar-x4.c b/src/f32-vbinary/vsubc-scalar-x4.c
similarity index 97%
rename from src/f32-binop/vsubc-scalar-x4.c
rename to src/f32-vbinary/vsubc-scalar-x4.c
index ce7dd54..1095de8 100644
--- a/src/f32-binop/vsubc-scalar-x4.c
+++ b/src/f32-vbinary/vsubc-scalar-x4.c
@@ -11,7 +11,7 @@
#include <xnnpack/common.h>
#include <xnnpack/math.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsubc_ukernel__scalar_x4(
diff --git a/src/f32-binop/vsubc-sse-x4.c b/src/f32-vbinary/vsubc-sse-x4.c
similarity index 97%
rename from src/f32-binop/vsubc-sse-x4.c
rename to src/f32-vbinary/vsubc-sse-x4.c
index 9cf424b..279e884 100644
--- a/src/f32-binop/vsubc-sse-x4.c
+++ b/src/f32-vbinary/vsubc-sse-x4.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsubc_ukernel__sse_x4(
diff --git a/src/f32-binop/vsubc-sse-x8.c b/src/f32-vbinary/vsubc-sse-x8.c
similarity index 98%
rename from src/f32-binop/vsubc-sse-x8.c
rename to src/f32-vbinary/vsubc-sse-x8.c
index bc81a8e..caa16e9 100644
--- a/src/f32-binop/vsubc-sse-x8.c
+++ b/src/f32-vbinary/vsubc-sse-x8.c
@@ -12,7 +12,7 @@
#include <xmmintrin.h>
#include <xnnpack/common.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
void xnn_f32_vsubc_ukernel__sse_x8(
diff --git a/src/init.c b/src/init.c
index fc15c32..b5795af 100644
--- a/src/init.c
+++ b/src/init.c
@@ -41,9 +41,9 @@
#include <xnnpack/spmm.h>
#include <xnnpack/unpool.h>
#include <xnnpack/vadd.h>
-#include <xnnpack/vbinop.h>
+#include <xnnpack/vbinary.h>
#include <xnnpack/vmulcaddc.h>
-#include <xnnpack/vunop.h>
+#include <xnnpack/vunary.h>
#include <xnnpack/zip.h>
#ifndef XNN_ENABLE_ASSEMBLY
@@ -208,10 +208,10 @@
.channel_tile = 8,
};
xnn_params.f32.vadd = (xnn_vadd_ukernel_function) xnn_f32_vadd_ukernel__neon_x8;
- xnn_params.f32.vmul = (struct vbinop_parameters) {
- .op_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmul_ukernel__neon_x8,
- .opc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__neon_x8,
- .ropc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__neon_x8,
+ xnn_params.f32.vmul = (struct vbinary_parameters) {
+ .op_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmul_ukernel__neon_x8,
+ .opc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__neon_x8,
+ .ropc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__neon_x8,
.element_tile = 8,
};
xnn_params.f32.vmulcaddc = (struct vmulcaddc_parameters) {
@@ -483,10 +483,10 @@
.channel_tile = 8,
};
xnn_params.f32.vadd = (xnn_vadd_ukernel_function) xnn_f32_vadd_ukernel__neon_x8;
- xnn_params.f32.vmul = (struct vbinop_parameters) {
- .op_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmul_ukernel__neon_x8,
- .opc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__neon_x8,
- .ropc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__neon_x8,
+ xnn_params.f32.vmul = (struct vbinary_parameters) {
+ .op_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmul_ukernel__neon_x8,
+ .opc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__neon_x8,
+ .ropc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__neon_x8,
.element_tile = 8,
};
xnn_params.f32.vmulcaddc = (struct vmulcaddc_parameters) {
@@ -721,10 +721,10 @@
.channel_tile = 8,
};
xnn_params.f32.vadd = (xnn_vadd_ukernel_function) xnn_f32_vadd_ukernel__sse_x8;
- xnn_params.f32.vmul = (struct vbinop_parameters) {
- .op_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmul_ukernel__sse_x8,
- .opc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__sse_x8,
- .ropc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__sse_x8,
+ xnn_params.f32.vmul = (struct vbinary_parameters) {
+ .op_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmul_ukernel__sse_x8,
+ .opc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__sse_x8,
+ .ropc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__sse_x8,
.element_tile = 8,
};
xnn_params.f32.vmulcaddc = (struct vmulcaddc_parameters) {
@@ -922,10 +922,10 @@
.channel_tile = 8,
};
xnn_params.f32.vadd = (xnn_vadd_ukernel_function) xnn_f32_vadd_ukernel__psimd_x8;
- xnn_params.f32.vmul = (struct vbinop_parameters) {
- .op_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmul_ukernel__psimd_x8,
- .opc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__psimd_x8,
- .ropc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__psimd_x8,
+ xnn_params.f32.vmul = (struct vbinary_parameters) {
+ .op_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmul_ukernel__psimd_x8,
+ .opc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__psimd_x8,
+ .ropc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__psimd_x8,
.element_tile = 8,
};
xnn_params.f32.vmulcaddc = (struct vmulcaddc_parameters) {
@@ -1098,10 +1098,10 @@
.channel_tile = 4,
};
xnn_params.f32.vadd = (xnn_vadd_ukernel_function) xnn_f32_vadd_ukernel__scalar_x4;
- xnn_params.f32.vmul = (struct vbinop_parameters) {
- .op_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmul_ukernel__scalar_x4,
- .opc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__scalar_x4,
- .ropc_ukernel = (xnn_vbinop_ukernel_function) xnn_f32_vmulc_ukernel__scalar_x4,
+ xnn_params.f32.vmul = (struct vbinary_parameters) {
+ .op_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmul_ukernel__scalar_x4,
+ .opc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__scalar_x4,
+ .ropc_ukernel = (xnn_vbinary_ukernel_function) xnn_f32_vmulc_ukernel__scalar_x4,
.element_tile = 8,
};
xnn_params.f32.vmulcaddc = (struct vmulcaddc_parameters) {
diff --git a/src/xnnpack/compute.h b/src/xnnpack/compute.h
index 8eb4fa4..4f2833a 100644
--- a/src/xnnpack/compute.h
+++ b/src/xnnpack/compute.h
@@ -583,7 +583,7 @@
union xnn_q8_add_params q8;
union xnn_f32_output_params f32;
} params;
- xnn_vbinop_ukernel_function ukernel;
+ xnn_vbinary_ukernel_function ukernel;
};
#ifndef __cplusplus
diff --git a/src/xnnpack/params.h b/src/xnnpack/params.h
index c76315e..87625eb 100644
--- a/src/xnnpack/params.h
+++ b/src/xnnpack/params.h
@@ -1076,27 +1076,27 @@
uint8_t* y,
const union xnn_q8_add_params* params);
-typedef void (*xnn_vbinop_ukernel_function)(
+typedef void (*xnn_vbinary_ukernel_function)(
size_t n,
const void* a,
const void* b,
void* y,
const void* params);
-typedef void (*xnn_f32_vbinop_ukernel_function)(
+typedef void (*xnn_f32_vbinary_ukernel_function)(
size_t n,
const float* a,
const float* b,
float* y,
const union xnn_f32_output_params* params);
-typedef void (*xnn_vunop_ukernel_function)(
+typedef void (*xnn_vunary_ukernel_function)(
size_t n,
const void* x,
void* y,
const void* params);
-typedef void (*xnn_f32_vunop_ukernel_function)(
+typedef void (*xnn_f32_vunary_ukernel_function)(
size_t n,
const float* x,
float* y,
@@ -1195,10 +1195,10 @@
uint8_t log2_sr;
};
-struct vbinop_parameters {
- xnn_vbinop_ukernel_function op_ukernel;
- xnn_vbinop_ukernel_function opc_ukernel;
- xnn_vbinop_ukernel_function ropc_ukernel;
+struct vbinary_parameters {
+ xnn_vbinary_ukernel_function op_ukernel;
+ xnn_vbinary_ukernel_function opc_ukernel;
+ xnn_vbinary_ukernel_function ropc_ukernel;
// Number of elements in a tile.
// For best efficiency, micro-kernel must process a multiple of this number of elements in each call.
uint8_t element_tile;
@@ -1363,7 +1363,7 @@
xnn_univector_ukernel_function sigmoid;
struct prelu_parameters prelu;
xnn_vadd_ukernel_function vadd;
- struct vbinop_parameters vmul;
+ struct vbinary_parameters vmul;
struct vmulcaddc_parameters vmulcaddc;
// Sparse Matrix-Dense Matrix Multiplication (NR=1 block).
struct spmm_parameters spmm;
diff --git a/src/xnnpack/vbinop.h b/src/xnnpack/vbinary.h
similarity index 100%
rename from src/xnnpack/vbinop.h
rename to src/xnnpack/vbinary.h
diff --git a/src/xnnpack/vunary.h b/src/xnnpack/vunary.h
new file mode 100644
index 0000000..46de442
--- /dev/null
+++ b/src/xnnpack/vunary.h
@@ -0,0 +1,35 @@
+// Copyright 2019 Google LLC
+//
+// This source code is licensed under the BSD-style license found in the
+// LICENSE file in the root directory of this source tree.
+
+#pragma once
+
+#include <stddef.h>
+#include <stdint.h>
+
+#include <xnnpack/params.h>
+#include <xnnpack/common.h>
+
+#ifdef __cplusplus
+extern "C" {
+#endif
+
+
+#define DECLARE_F32_VUNARY_UKERNEL_FUNCTION(fn_name) \
+ XNN_INTERNAL void fn_name( \
+ size_t n, \
+ const float* x, \
+ float* y, \
+ const void* params);
+
+DECLARE_F32_VUNARY_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__neonfma_p5_nr2fma_x16)
+DECLARE_F32_VUNARY_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__neon_frac_p9_p10_nr1recps_x16)
+DECLARE_F32_VUNARY_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__sse2_p5_div_x8)
+DECLARE_F32_VUNARY_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__sse2_p5_div_x16)
+DECLARE_F32_VUNARY_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__sse41_p5_div_x8)
+DECLARE_F32_VUNARY_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__sse41_p5_div_x16)
+
+#ifdef __cplusplus
+} // extern "C"
+#endif
diff --git a/src/xnnpack/vunop.h b/src/xnnpack/vunop.h
deleted file mode 100644
index 86b0723..0000000
--- a/src/xnnpack/vunop.h
+++ /dev/null
@@ -1,36 +0,0 @@
-// Copyright 2019 Google LLC
-//
-// This source code is licensed under the BSD-style license found in the
-// LICENSE file in the root directory of this source tree.
-
-#pragma once
-
-#include <stddef.h>
-#include <stdint.h>
-
-#include <xnnpack/params.h>
-#include <xnnpack/common.h>
-
-#ifdef __cplusplus
-extern "C" {
-#endif
-
-
-#define DECLARE_F32_VUNOP_UKERNEL_FUNCTION(fn_name) \
- XNN_INTERNAL void fn_name( \
- size_t n, \
- const float* x, \
- float* y, \
- const void* params);
-
-DECLARE_F32_VUNOP_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__neonfma_p5_nr2fma_x16)
-DECLARE_F32_VUNOP_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__neon_frac_p9_p10_nr1recps_x16)
-DECLARE_F32_VUNOP_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__sse2_p5_div_x8)
-DECLARE_F32_VUNOP_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__sse2_p5_div_x16)
-DECLARE_F32_VUNOP_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__sse41_p5_div_x8)
-DECLARE_F32_VUNOP_UKERNEL_FUNCTION(xnn_f32_sigmoid_ukernel__sse41_p5_div_x16)
-
-
-#ifdef __cplusplus
-} // extern "C"
-#endif