xref: /aosp_15_r20/external/XNNPACK/src/f32-vscaleexpminusmax/avx512f-p5-scalef.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 % 16 == 0
7*4bdc9457SAndroid Build Coastguard Worker$assert ELEMENTS_TILE >= 16
8*4bdc9457SAndroid Build Coastguard Worker$SIMD_TILE = ELEMENTS_TILE // 16
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/intrinsics-polyfill.h>
15*4bdc9457SAndroid Build Coastguard Worker#include <xnnpack/vscaleexpminusmax.h>
16*4bdc9457SAndroid Build Coastguard Worker
17*4bdc9457SAndroid Build Coastguard Worker
18*4bdc9457SAndroid Build Coastguard Workervoid xnn_f32_vscaleexpminusmax_ukernel__avx512f_p5_scalef_x${ELEMENTS_TILE}(
19*4bdc9457SAndroid Build Coastguard Worker    size_t elements,
20*4bdc9457SAndroid Build Coastguard Worker    const float* input,
21*4bdc9457SAndroid Build Coastguard Worker    float* output,
22*4bdc9457SAndroid Build Coastguard Worker    float scale,
23*4bdc9457SAndroid Build Coastguard Worker    float max)
24*4bdc9457SAndroid Build Coastguard Worker{
25*4bdc9457SAndroid Build Coastguard Worker  assert(elements % sizeof(float) == 0);
26*4bdc9457SAndroid Build Coastguard Worker
27*4bdc9457SAndroid Build Coastguard Worker  const __m512 vlog2e = _mm512_set1_ps(0x1.715476p+0f);
28*4bdc9457SAndroid Build Coastguard Worker  const __m512 vminus_ln2_hi = _mm512_set1_ps(-0x1.62E43p-1f);
29*4bdc9457SAndroid Build Coastguard Worker  const __m512 vminus_ln2_lo = _mm512_set1_ps(0x1.05C61p-29f);
30*4bdc9457SAndroid Build Coastguard Worker
31*4bdc9457SAndroid Build Coastguard Worker  const __m512 vc0 = _mm512_set1_ps(1.0f);
32*4bdc9457SAndroid Build Coastguard Worker  const __m512 vc1 = _mm512_set1_ps(0x1.FFFFF6p-1f);
33*4bdc9457SAndroid Build Coastguard Worker  const __m512 vc2 = _mm512_set1_ps(0x1.FFFDC6p-2f);
34*4bdc9457SAndroid Build Coastguard Worker  const __m512 vc3 = _mm512_set1_ps(0x1.555A80p-3f);
35*4bdc9457SAndroid Build Coastguard Worker  const __m512 vc4 = _mm512_set1_ps(0x1.573A1Ap-5f);
36*4bdc9457SAndroid Build Coastguard Worker  const __m512 vc5 = _mm512_set1_ps(0x1.0F9F9Cp-7f);
37*4bdc9457SAndroid Build Coastguard Worker
38*4bdc9457SAndroid Build Coastguard Worker  const __m512 vscale = _mm512_set1_ps(scale);
39*4bdc9457SAndroid Build Coastguard Worker  const __m512 vi_max = _mm512_set1_ps(max);
40*4bdc9457SAndroid Build Coastguard Worker
41*4bdc9457SAndroid Build Coastguard Worker  for (; elements >= ${ELEMENTS_TILE} * sizeof(float); elements -= ${ELEMENTS_TILE} * sizeof(float)) {
42*4bdc9457SAndroid Build Coastguard Worker    // Load ${ELEMENTS_TILE} (${SIMD_TILE}x16) inputs at a time.
43*4bdc9457SAndroid Build Coastguard Worker    const __m512 vi0 = _mm512_loadu_ps(input);
44*4bdc9457SAndroid Build Coastguard Worker    $for N in range(1, SIMD_TILE):
45*4bdc9457SAndroid Build Coastguard Worker      const __m512 vi${N} = _mm512_loadu_ps(input + ${N * 16});
46*4bdc9457SAndroid Build Coastguard Worker    input += ${ELEMENTS_TILE};
47*4bdc9457SAndroid Build Coastguard Worker
48*4bdc9457SAndroid Build Coastguard Worker    // Subtract maximum input x := i - i_max.
49*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
50*4bdc9457SAndroid Build Coastguard Worker      const __m512 vx${N} = _mm512_sub_ps(vi${N}, vi_max);
51*4bdc9457SAndroid Build Coastguard Worker
52*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument elements := round(x / log(2)).
53*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
54*4bdc9457SAndroid Build Coastguard Worker      __m512 vn${N} = _mm512_roundscale_ps(_mm512_mul_ps(vx${N}, vlog2e), 0);
55*4bdc9457SAndroid Build Coastguard Worker
56*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument t := x - elements * log(2).
57*4bdc9457SAndroid Build Coastguard Worker    // Use Cody-Waite range reduction method (note two constants to represent log(2)) to improve accuracy.
58*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
59*4bdc9457SAndroid Build Coastguard Worker      __m512 vt${N} = _mm512_fmadd_ps(vn${N}, vminus_ln2_hi, vx${N});
60*4bdc9457SAndroid Build Coastguard Worker
61*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
62*4bdc9457SAndroid Build Coastguard Worker      vt${N} = _mm512_fmadd_ps(vn${N}, vminus_ln2_lo, vt${N});
63*4bdc9457SAndroid Build Coastguard Worker
64*4bdc9457SAndroid Build Coastguard Worker    // Compute degree-5 polynomial approximation for exp(t) on [-log(2)/2, log(2)/2].
65*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
66*4bdc9457SAndroid Build Coastguard Worker      __m512 vp${N} = _mm512_fmadd_ps(vc5, vt${N}, vc4);
67*4bdc9457SAndroid Build Coastguard Worker
68*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
69*4bdc9457SAndroid Build Coastguard Worker      vp${N} = _mm512_fmadd_ps(vp${N}, vt${N}, vc3);
70*4bdc9457SAndroid Build Coastguard Worker
71*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
72*4bdc9457SAndroid Build Coastguard Worker      vp${N} = _mm512_fmadd_ps(vp${N}, vt${N}, vc2);
73*4bdc9457SAndroid Build Coastguard Worker
74*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
75*4bdc9457SAndroid Build Coastguard Worker      vp${N} = _mm512_fmadd_ps(vp${N}, vt${N}, vc1);
76*4bdc9457SAndroid Build Coastguard Worker
77*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
78*4bdc9457SAndroid Build Coastguard Worker      vp${N} = _mm512_fmadd_ps(vp${N}, vt${N}, vc0);
79*4bdc9457SAndroid Build Coastguard Worker
80*4bdc9457SAndroid Build Coastguard Worker    // Reconstruct the final f value:
81*4bdc9457SAndroid Build Coastguard Worker    //   f = 2**elements * (1 + t * (c1 + t * (c2 + t * (c3 + t * (c4 + t * c5)))))
82*4bdc9457SAndroid Build Coastguard Worker    //     = 2**elements * p
83*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
84*4bdc9457SAndroid Build Coastguard Worker      __m512 vf${N} = _mm512_scalef_ps(vp${N}, vn${N});
85*4bdc9457SAndroid Build Coastguard Worker
86*4bdc9457SAndroid Build Coastguard Worker    // Multiply by scale.
87*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
88*4bdc9457SAndroid Build Coastguard Worker      vf${N} = _mm512_mul_ps(vf${N}, vscale);
89*4bdc9457SAndroid Build Coastguard Worker
90*4bdc9457SAndroid Build Coastguard Worker    // Store ${ELEMENTS_TILE} (${SIMD_TILE}x16) outputs at a time.
91*4bdc9457SAndroid Build Coastguard Worker    _mm512_storeu_ps(output, vf0);
92*4bdc9457SAndroid Build Coastguard Worker    $for N in range(SIMD_TILE):
93*4bdc9457SAndroid Build Coastguard Worker      _mm512_storeu_ps(output + ${N * 16}, vf${N});
94*4bdc9457SAndroid Build Coastguard Worker    output += ${ELEMENTS_TILE};
95*4bdc9457SAndroid Build Coastguard Worker  }
96*4bdc9457SAndroid Build Coastguard Worker  for (; elements >= 16 * sizeof(float); elements -= 16 * sizeof(float)) {
97*4bdc9457SAndroid Build Coastguard Worker    // Load 16 inputs at a time.
98*4bdc9457SAndroid Build Coastguard Worker    const __m512 vi = _mm512_loadu_ps(input);
99*4bdc9457SAndroid Build Coastguard Worker    input += 16;
100*4bdc9457SAndroid Build Coastguard Worker
101*4bdc9457SAndroid Build Coastguard Worker    // Subtract maximum input x := i - i_max.
102*4bdc9457SAndroid Build Coastguard Worker    const __m512 vx = _mm512_sub_ps(vi, vi_max);
103*4bdc9457SAndroid Build Coastguard Worker
104*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument elements := round(x / log(2)).
105*4bdc9457SAndroid Build Coastguard Worker    __m512 vn = _mm512_roundscale_ps(_mm512_mul_ps(vx, vlog2e), 0);
106*4bdc9457SAndroid Build Coastguard Worker
107*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument t := x - elements * log(2).
108*4bdc9457SAndroid Build Coastguard Worker    // Use Cody-Waite range reduction method (note two constants to represent log(2)) to improve accuracy.
109*4bdc9457SAndroid Build Coastguard Worker    __m512 vt = _mm512_fmadd_ps(vn, vminus_ln2_hi, vx);
110*4bdc9457SAndroid Build Coastguard Worker    vt = _mm512_fmadd_ps(vn, vminus_ln2_lo, vt);
111*4bdc9457SAndroid Build Coastguard Worker
112*4bdc9457SAndroid Build Coastguard Worker    // Compute degree-5 polynomial approximation for exp(t) on [-log(2)/2, log(2)/2].
113*4bdc9457SAndroid Build Coastguard Worker    __m512 vp = _mm512_fmadd_ps(vc5, vt, vc4);
114*4bdc9457SAndroid Build Coastguard Worker    vp = _mm512_fmadd_ps(vp, vt, vc3);
115*4bdc9457SAndroid Build Coastguard Worker    vp = _mm512_fmadd_ps(vp, vt, vc2);
116*4bdc9457SAndroid Build Coastguard Worker    vp = _mm512_fmadd_ps(vp, vt, vc1);
117*4bdc9457SAndroid Build Coastguard Worker    vp = _mm512_fmadd_ps(vp, vt, vc0);
118*4bdc9457SAndroid Build Coastguard Worker
119*4bdc9457SAndroid Build Coastguard Worker    // Reconstruct the final f value:
120*4bdc9457SAndroid Build Coastguard Worker    //   f = 2**elements * (1 + t * (c1 + t * (c2 + t * (c3 + t * (c4 + t * c5)))))
121*4bdc9457SAndroid Build Coastguard Worker    //     = 2**elements * p
122*4bdc9457SAndroid Build Coastguard Worker    __m512 vf = _mm512_scalef_ps(vp, vn);
123*4bdc9457SAndroid Build Coastguard Worker
124*4bdc9457SAndroid Build Coastguard Worker    // Multiply by scale.
125*4bdc9457SAndroid Build Coastguard Worker    vf = _mm512_mul_ps(vf, vscale);
126*4bdc9457SAndroid Build Coastguard Worker
127*4bdc9457SAndroid Build Coastguard Worker    // Store 16 outputs at a time.
128*4bdc9457SAndroid Build Coastguard Worker    _mm512_storeu_ps(output, vf);
129*4bdc9457SAndroid Build Coastguard Worker    output += 16;
130*4bdc9457SAndroid Build Coastguard Worker  }
131*4bdc9457SAndroid Build Coastguard Worker  if (elements != 0) {
132*4bdc9457SAndroid Build Coastguard Worker    // Prepare mask for valid 32-bit elements (depends on elements).
133*4bdc9457SAndroid Build Coastguard Worker    elements >>= 2 /* log2(sizeof(float)) */;
134*4bdc9457SAndroid Build Coastguard Worker    const __mmask16 vmask = _cvtu32_mask16((uint16_t) ((uint32_t) (UINT32_C(1) << elements) - UINT32_C(1)));
135*4bdc9457SAndroid Build Coastguard Worker
136*4bdc9457SAndroid Build Coastguard Worker    // Load up to 15 inputs at a time.
137*4bdc9457SAndroid Build Coastguard Worker    const __m512 vi = _mm512_mask_loadu_ps(_mm512_undefined_ps(), vmask, input);
138*4bdc9457SAndroid Build Coastguard Worker
139*4bdc9457SAndroid Build Coastguard Worker    // Subtract maximum input x := i - i_max.
140*4bdc9457SAndroid Build Coastguard Worker    const __m512 vx = _mm512_sub_ps(vi, vi_max);
141*4bdc9457SAndroid Build Coastguard Worker
142*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument elements := round(x / log(2)).
143*4bdc9457SAndroid Build Coastguard Worker    __m512 vn = _mm512_roundscale_ps(_mm512_mul_ps(vx, vlog2e), 0);
144*4bdc9457SAndroid Build Coastguard Worker
145*4bdc9457SAndroid Build Coastguard Worker    // Compute reduced argument t := x - elements * log(2).
146*4bdc9457SAndroid Build Coastguard Worker    // Use Cody-Waite range reduction method (note two constants to represent log(2)) to improve accuracy.
147*4bdc9457SAndroid Build Coastguard Worker    __m512 vt = _mm512_fmadd_ps(vn, vminus_ln2_hi, vx);
148*4bdc9457SAndroid Build Coastguard Worker    vt = _mm512_fmadd_ps(vn, vminus_ln2_lo, vt);
149*4bdc9457SAndroid Build Coastguard Worker
150*4bdc9457SAndroid Build Coastguard Worker    // Compute degree-5 polynomial approximation for exp(t) on [-log(2)/2, log(2)/2].
151*4bdc9457SAndroid Build Coastguard Worker    __m512 vp = _mm512_fmadd_ps(vc5, vt, vc4);
152*4bdc9457SAndroid Build Coastguard Worker    vp = _mm512_fmadd_ps(vp, vt, vc3);
153*4bdc9457SAndroid Build Coastguard Worker    vp = _mm512_fmadd_ps(vp, vt, vc2);
154*4bdc9457SAndroid Build Coastguard Worker    vp = _mm512_fmadd_ps(vp, vt, vc1);
155*4bdc9457SAndroid Build Coastguard Worker    vp = _mm512_fmadd_ps(vp, vt, vc0);
156*4bdc9457SAndroid Build Coastguard Worker
157*4bdc9457SAndroid Build Coastguard Worker    // Reconstruct the final f value:
158*4bdc9457SAndroid Build Coastguard Worker    //   f = 2**elements * (1 + t * (c1 + t * (c2 + t * (c3 + t * (c4 + t * c5)))))
159*4bdc9457SAndroid Build Coastguard Worker    //     = 2**elements * p
160*4bdc9457SAndroid Build Coastguard Worker    __m512 vf = _mm512_scalef_ps(vp, vn);
161*4bdc9457SAndroid Build Coastguard Worker
162*4bdc9457SAndroid Build Coastguard Worker    // Multiply by scale.
163*4bdc9457SAndroid Build Coastguard Worker    vf = _mm512_mul_ps(vf, vscale);
164*4bdc9457SAndroid Build Coastguard Worker
165*4bdc9457SAndroid Build Coastguard Worker    // Store up to 15 outputs at a time.
166*4bdc9457SAndroid Build Coastguard Worker    _mm512_mask_storeu_ps(output, vmask, vf);
167*4bdc9457SAndroid Build Coastguard Worker  }
168*4bdc9457SAndroid Build Coastguard Worker}
169