xref: /aosp_15_r20/external/XNNPACK/src/f32-vscaleextexp/avx2-p5.c.in (revision 4bdc94577ba0e567308109d787f7fec7b531ce36)
1*4bdc9457SAndroid Build Coastguard Worker// Copyright 2019 Google LLC
2*4bdc9457SAndroid Build Coastguard Worker//
3*4bdc9457SAndroid Build Coastguard Worker// This source code is licensed under the BSD-style license found in the
4*4bdc9457SAndroid Build Coastguard Worker// LICENSE file in the root directory of this source tree.
5*4bdc9457SAndroid Build Coastguard Worker
6*4bdc9457SAndroid Build Coastguard Worker$assert ELEMENTS_TILE % 8 == 0
7*4bdc9457SAndroid Build Coastguard Worker$assert ELEMENTS_TILE >= 8
8*4bdc9457SAndroid Build Coastguard Worker$SIMD_TILE = ELEMENTS_TILE // 8
9*4bdc9457SAndroid Build Coastguard Worker$ABC = "0123456789ABCDEFGHIJKLMNOPQRSTUVWXYZ"
10*4bdc9457SAndroid Build Coastguard Worker#include <assert.h>
11*4bdc9457SAndroid Build Coastguard Worker
12*4bdc9457SAndroid Build Coastguard Worker#include <immintrin.h>
13*4bdc9457SAndroid Build Coastguard Worker
14*4bdc9457SAndroid Build Coastguard Worker#include <xnnpack/common.h>
15*4bdc9457SAndroid Build Coastguard Worker#include <xnnpack/vscaleextexp.h>
16*4bdc9457SAndroid Build Coastguard Worker
17*4bdc9457SAndroid Build Coastguard Worker
18*4bdc9457SAndroid Build Coastguard Workerstatic const int32_t mask_table[14] = {-1, -1, -1, -1, -1, -1, -1, 0, 0, 0, 0, 0, 0, 0};
19*4bdc9457SAndroid Build Coastguard Worker
20*4bdc9457SAndroid Build Coastguard Workervoid xnn_f32_vscaleextexp_ukernel__avx2_p5_x${ELEMENTS_TILE}(
21*4bdc9457SAndroid Build Coastguard Worker    size_t elements,
22*4bdc9457SAndroid Build Coastguard Worker    const float* x,
23*4bdc9457SAndroid Build Coastguard Worker    float* y,
24*4bdc9457SAndroid Build Coastguard Worker    float scale_value,
25*4bdc9457SAndroid Build Coastguard Worker    float scale_exp)
26*4bdc9457SAndroid Build Coastguard Worker{
27*4bdc9457SAndroid Build Coastguard Worker  assert(elements % sizeof(float) == 0);
28*4bdc9457SAndroid Build Coastguard Worker
29*4bdc9457SAndroid Build Coastguard Worker  const __m256 vlog2e = _mm256_set1_ps(0x1.715476p+0f);
30*4bdc9457SAndroid Build Coastguard Worker  const __m256 vminus_ln2_hi = _mm256_set1_ps(-0x1.62E43p-1f);
31*4bdc9457SAndroid Build Coastguard Worker  const __m256 vminus_ln2_lo = _mm256_set1_ps(0x1.05C61p-29f);
32*4bdc9457SAndroid Build Coastguard Worker
33*4bdc9457SAndroid Build Coastguard Worker  // The smallest elements such that 2**elements is considered non-negligible.
34*4bdc9457SAndroid Build Coastguard Worker  // For smaller elements, 2**elements is replaced with zero.
35*4bdc9457SAndroid Build Coastguard Worker  const __m256 vmin_exponent = _mm256_set1_ps(-127.0f);
36*4bdc9457SAndroid Build Coastguard Worker  const __m256 vmagic_bias = _mm256_set1_ps(0x1.8000FEp23f);
37*4bdc9457SAndroid Build Coastguard Worker
38*4bdc9457SAndroid Build Coastguard Worker  const __m256 vc0 = _mm256_set1_ps(1.0f);
39*4bdc9457SAndroid Build Coastguard Worker  const __m256 vc1 = _mm256_set1_ps(0x1.FFFFF6p-1f);
40*4bdc9457SAndroid Build Coastguard Worker  const __m256 vc2 = _mm256_set1_ps(0x1.FFFDC6p-2f);
41*4bdc9457SAndroid Build Coastguard Worker  const __m256 vc3 = _mm256_set1_ps(0x1.555A80p-3f);
42*4bdc9457SAndroid Build Coastguard Worker  const __m256 vc4 = _mm256_set1_ps(0x1.573A1Ap-5f);
43*4bdc9457SAndroid Build Coastguard Worker  const __m256 vc5 = _mm256_set1_ps(0x1.0F9F9Cp-7f);
44*4bdc9457SAndroid Build Coastguard Worker
45*4bdc9457SAndroid Build Coastguard Worker  const __m256 vscalev = _mm256_set1_ps(scale_value);
46*4bdc9457SAndroid Build Coastguard Worker  const __m256 vscalee = _mm256_set1_ps(scale_exp);
47*4bdc9457SAndroid Build Coastguard Worker
48*4bdc9457SAndroid Build Coastguard Worker  for (; elements >= ${ELEMENTS_TILE} * sizeof(float); elements -= ${ELEMENTS_TILE} * sizeof(float)) {
49*4bdc9457SAndroid Build Coastguard Worker    // Load ${ELEMENTS_TILE} (${SIMD_TILE}x8) inputs at a time.
50*4bdc9457SAndroid Build Coastguard Worker    const __m256 vx0 = _mm256_loadu_ps(x);
51*4bdc9457SAndroid Build Coastguard Worker    $for N in range(1, SIMD_TILE):
52*4bdc9457SAndroid Build Coastguard Worker      const __m256 vx${N} = _mm256_loadu_ps(x + ${N * 8});
53*4bdc9457SAndroid Build Coastguard Worker    x += ${ELEMENTS_TILE};
54*4bdc9457SAndroid Build Coastguard Worker
55*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument elements := round(x / log(2)).
56*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
57*4bdc9457SAndroid Build Coastguard Worker      const __m256 vn${N} = _mm256_round_ps(_mm256_mul_ps(vx${N}, vlog2e), _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC);
58*4bdc9457SAndroid Build Coastguard Worker
59*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument t := x - elements * log(2).
60*4bdc9457SAndroid Build Coastguard Worker    // Use Cody-Waite range reduction method (note two constants to represent log(2)) to improve accuracy.
61*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
62*4bdc9457SAndroid Build Coastguard Worker      __m256 vt${N} = _mm256_fmadd_ps(vn${N}, vminus_ln2_hi, vx${N});
63*4bdc9457SAndroid Build Coastguard Worker
64*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
65*4bdc9457SAndroid Build Coastguard Worker      vt${N} = _mm256_fmadd_ps(vn${N}, vminus_ln2_lo, vt${N});
66*4bdc9457SAndroid Build Coastguard Worker
67*4bdc9457SAndroid Build Coastguard Worker    // Compute degree-5 polynomial approximation for exp(t) on [-log(2)/2, log(2)/2].
68*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
69*4bdc9457SAndroid Build Coastguard Worker      __m256 vp${N} = _mm256_fmadd_ps(vc5, vt${N}, vc4);
70*4bdc9457SAndroid Build Coastguard Worker
71*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
72*4bdc9457SAndroid Build Coastguard Worker      vp${N} = _mm256_fmadd_ps(vp${N}, vt${N}, vc3);
73*4bdc9457SAndroid Build Coastguard Worker
74*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
75*4bdc9457SAndroid Build Coastguard Worker      vp${N} = _mm256_fmadd_ps(vp${N}, vt${N}, vc2);
76*4bdc9457SAndroid Build Coastguard Worker
77*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
78*4bdc9457SAndroid Build Coastguard Worker      vp${N} = _mm256_fmadd_ps(vp${N}, vt${N}, vc1);
79*4bdc9457SAndroid Build Coastguard Worker
80*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
81*4bdc9457SAndroid Build Coastguard Worker      vp${N} = _mm256_fmadd_ps(vp${N}, vt${N}, vc0);
82*4bdc9457SAndroid Build Coastguard Worker
83*4bdc9457SAndroid Build Coastguard Worker    // Multiply "extended" floating-point numbers in ("mantissa", "exponent") representation where
84*4bdc9457SAndroid Build Coastguard Worker    //  - vnX is "exponent"
85*4bdc9457SAndroid Build Coastguard Worker    //  - vpX is "mantissa"
86*4bdc9457SAndroid Build Coastguard Worker    //
87*4bdc9457SAndroid Build Coastguard Worker    // exp2(ae) * av * exp2(be) * bv =
88*4bdc9457SAndroid Build Coastguard Worker    //   = exp2(ae + be) * (av * bv)
89*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
90*4bdc9457SAndroid Build Coastguard Worker      __m256 vf${N} = _mm256_mul_ps(vp${N}, vscalev);
91*4bdc9457SAndroid Build Coastguard Worker
92*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
93*4bdc9457SAndroid Build Coastguard Worker      __m256 ve${N} = _mm256_add_ps(vn${N}, vscalee);
94*4bdc9457SAndroid Build Coastguard Worker
95*4bdc9457SAndroid Build Coastguard Worker    // For computational efficiency, replace exp2(e) with 0.0f when e <= -127.0.
96*4bdc9457SAndroid Build Coastguard Worker    // This replacement is done in two steps:
97*4bdc9457SAndroid Build Coastguard Worker    // 1. Clamp minimum e at -127.0.
98*4bdc9457SAndroid Build Coastguard Worker    // 2. Map e to scale factor 0.0 when e == -127.0
99*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
100*4bdc9457SAndroid Build Coastguard Worker      ve${N} = _mm256_max_ps(ve${N}, vmin_exponent);
101*4bdc9457SAndroid Build Coastguard Worker
102*4bdc9457SAndroid Build Coastguard Worker    // Convert exponents into scale factors:
103*4bdc9457SAndroid Build Coastguard Worker    // - s = exp2(e) when e > -127.0
104*4bdc9457SAndroid Build Coastguard Worker    // - s = 0.0 when e <= -127.0
105*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
106*4bdc9457SAndroid Build Coastguard Worker      const __m256 vs${N} = _mm256_castsi256_ps(_mm256_slli_epi32(_mm256_castps_si256(_mm256_add_ps(ve${N}, vmagic_bias)), 23));
107*4bdc9457SAndroid Build Coastguard Worker
108*4bdc9457SAndroid Build Coastguard Worker    // Multiply "mantissa" by the scale factor.
109*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
110*4bdc9457SAndroid Build Coastguard Worker      vf${N} = _mm256_mul_ps(vf${N}, vs${N});
111*4bdc9457SAndroid Build Coastguard Worker
112*4bdc9457SAndroid Build Coastguard Worker    // Store ${ELEMENTS_TILE} (${SIMD_TILE}x8) outputs at a time.
113*4bdc9457SAndroid Build Coastguard Worker    _mm256_storeu_ps(y, vf0);
114*4bdc9457SAndroid Build Coastguard Worker    $for N in range(1, SIMD_TILE):
115*4bdc9457SAndroid Build Coastguard Worker      _mm256_storeu_ps(y + ${N * 8}, vf${N});
116*4bdc9457SAndroid Build Coastguard Worker    y += ${ELEMENTS_TILE};
117*4bdc9457SAndroid Build Coastguard Worker  }
118*4bdc9457SAndroid Build Coastguard Worker
119*4bdc9457SAndroid Build Coastguard Worker  for (; elements >= 8 * sizeof(float); elements -= 8 * sizeof(float)) {
120*4bdc9457SAndroid Build Coastguard Worker    // Load 8 inputs at a time.
121*4bdc9457SAndroid Build Coastguard Worker    const __m256 vx = _mm256_loadu_ps(x);
122*4bdc9457SAndroid Build Coastguard Worker    x += 8;
123*4bdc9457SAndroid Build Coastguard Worker
124*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument elements := round(x / log(2)).
125*4bdc9457SAndroid Build Coastguard Worker    const __m256 vn = _mm256_round_ps(_mm256_mul_ps(vx, vlog2e), _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC);
126*4bdc9457SAndroid Build Coastguard Worker
127*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument t := x - elements * log(2).
128*4bdc9457SAndroid Build Coastguard Worker    // Use Cody-Waite range reduction method (note two constants to represent log(2)) to improve accuracy.
129*4bdc9457SAndroid Build Coastguard Worker    __m256 vt = _mm256_fmadd_ps(vn, vminus_ln2_hi, vx);
130*4bdc9457SAndroid Build Coastguard Worker    vt = _mm256_fmadd_ps(vn, vminus_ln2_lo, vt);
131*4bdc9457SAndroid Build Coastguard Worker
132*4bdc9457SAndroid Build Coastguard Worker    // Compute degree-5 polynomial approximation for exp(t) on [-log(2)/2, log(2)/2].
133*4bdc9457SAndroid Build Coastguard Worker    __m256 vp = _mm256_fmadd_ps(vc5, vt, vc4);
134*4bdc9457SAndroid Build Coastguard Worker    vp = _mm256_fmadd_ps(vp, vt, vc3);
135*4bdc9457SAndroid Build Coastguard Worker    vp = _mm256_fmadd_ps(vp, vt, vc2);
136*4bdc9457SAndroid Build Coastguard Worker    vp = _mm256_fmadd_ps(vp, vt, vc1);
137*4bdc9457SAndroid Build Coastguard Worker    vp = _mm256_fmadd_ps(vp, vt, vc0);
138*4bdc9457SAndroid Build Coastguard Worker
139*4bdc9457SAndroid Build Coastguard Worker    // Multiply "extended" floating-point numbers in ("mantissa", "exponent") representation.
140*4bdc9457SAndroid Build Coastguard Worker    __m256 vf = _mm256_mul_ps(vp, vscalev);
141*4bdc9457SAndroid Build Coastguard Worker    __m256 ve = _mm256_add_ps(vn, vscalee);
142*4bdc9457SAndroid Build Coastguard Worker
143*4bdc9457SAndroid Build Coastguard Worker    // For computational efficiency, replace exp2(e) with 0.0f when e <= -127.0.
144*4bdc9457SAndroid Build Coastguard Worker    ve = _mm256_max_ps(ve, vmin_exponent);
145*4bdc9457SAndroid Build Coastguard Worker
146*4bdc9457SAndroid Build Coastguard Worker    // Convert exponents into scale factors.
147*4bdc9457SAndroid Build Coastguard Worker    const __m256 vs = _mm256_castsi256_ps(_mm256_slli_epi32(_mm256_castps_si256(_mm256_add_ps(ve, vmagic_bias)), 23));
148*4bdc9457SAndroid Build Coastguard Worker
149*4bdc9457SAndroid Build Coastguard Worker    // Multiply "mantissa" by the scale factor.
150*4bdc9457SAndroid Build Coastguard Worker    vf = _mm256_mul_ps(vf, vs);
151*4bdc9457SAndroid Build Coastguard Worker
152*4bdc9457SAndroid Build Coastguard Worker    // Store 8 results at a time.
153*4bdc9457SAndroid Build Coastguard Worker    _mm256_storeu_ps(y, vf);
154*4bdc9457SAndroid Build Coastguard Worker    y += 8;
155*4bdc9457SAndroid Build Coastguard Worker  }
156*4bdc9457SAndroid Build Coastguard Worker  if XNN_UNLIKELY(elements != 0) {
157*4bdc9457SAndroid Build Coastguard Worker    assert(elements >= 1 * sizeof(float));
158*4bdc9457SAndroid Build Coastguard Worker    assert(elements <= 7 * sizeof(float));
159*4bdc9457SAndroid Build Coastguard Worker    const __m256i vmask = _mm256_loadu_si256((const __m256i*) ((uintptr_t) &mask_table[7] - elements));
160*4bdc9457SAndroid Build Coastguard Worker
161*4bdc9457SAndroid Build Coastguard Worker    // Load up to 7 inputs at a time.
162*4bdc9457SAndroid Build Coastguard Worker    const __m256 vx = _mm256_maskload_ps(x, vmask);
163*4bdc9457SAndroid Build Coastguard Worker
164*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument elements := round(x / log(2)).
165*4bdc9457SAndroid Build Coastguard Worker    const __m256 vn = _mm256_round_ps(_mm256_mul_ps(vx, vlog2e), _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC);
166*4bdc9457SAndroid Build Coastguard Worker
167*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument t := x - elements * log(2).
168*4bdc9457SAndroid Build Coastguard Worker    // Use Cody-Waite range reduction method (note two constants to represent log(2)) to improve accuracy.
169*4bdc9457SAndroid Build Coastguard Worker    __m256 vt = _mm256_fmadd_ps(vn, vminus_ln2_hi, vx);
170*4bdc9457SAndroid Build Coastguard Worker    vt = _mm256_fmadd_ps(vn, vminus_ln2_lo, vt);
171*4bdc9457SAndroid Build Coastguard Worker
172*4bdc9457SAndroid Build Coastguard Worker    // Compute degree-5 polynomial approximation for exp(t) on [-log(2)/2, log(2)/2].
173*4bdc9457SAndroid Build Coastguard Worker    __m256 vp = _mm256_fmadd_ps(vc5, vt, vc4);
174*4bdc9457SAndroid Build Coastguard Worker    vp = _mm256_fmadd_ps(vp, vt, vc3);
175*4bdc9457SAndroid Build Coastguard Worker    vp = _mm256_fmadd_ps(vp, vt, vc2);
176*4bdc9457SAndroid Build Coastguard Worker    vp = _mm256_fmadd_ps(vp, vt, vc1);
177*4bdc9457SAndroid Build Coastguard Worker    vp = _mm256_fmadd_ps(vp, vt, vc0);
178*4bdc9457SAndroid Build Coastguard Worker
179*4bdc9457SAndroid Build Coastguard Worker    // Multiply "extended" floating-point numbers in ("mantissa", "exponent") representation.
180*4bdc9457SAndroid Build Coastguard Worker    __m256 vf = _mm256_mul_ps(vp, vscalev);
181*4bdc9457SAndroid Build Coastguard Worker    __m256 ve = _mm256_add_ps(vn, vscalee);
182*4bdc9457SAndroid Build Coastguard Worker
183*4bdc9457SAndroid Build Coastguard Worker    // For computational efficiency, replace exp2(e) with 0.0f when e <= -127.0.
184*4bdc9457SAndroid Build Coastguard Worker    ve = _mm256_max_ps(ve, vmin_exponent);
185*4bdc9457SAndroid Build Coastguard Worker
186*4bdc9457SAndroid Build Coastguard Worker    // Convert exponents into scale factors.
187*4bdc9457SAndroid Build Coastguard Worker    const __m256 vs = _mm256_castsi256_ps(_mm256_slli_epi32(_mm256_castps_si256(_mm256_add_ps(ve, vmagic_bias)), 23));
188*4bdc9457SAndroid Build Coastguard Worker
189*4bdc9457SAndroid Build Coastguard Worker    // Multiply "mantissa" by the scale factor.
190*4bdc9457SAndroid Build Coastguard Worker    vf = _mm256_mul_ps(vf, vs);
191*4bdc9457SAndroid Build Coastguard Worker
192*4bdc9457SAndroid Build Coastguard Worker    // Store up to 7 inputs at a time.
193*4bdc9457SAndroid Build Coastguard Worker    _mm256_maskstore_ps(y, vmask, vf);
194*4bdc9457SAndroid Build Coastguard Worker  }
195*4bdc9457SAndroid Build Coastguard Worker  _mm256_zeroupper();
196*4bdc9457SAndroid Build Coastguard Worker}
197