1*4bdc9457SAndroid Build Coastguard Worker// Copyright 2021 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 BATCH_TILE >= 16 7*4bdc9457SAndroid Build Coastguard Worker$assert BATCH_TILE % 16 == 0 8*4bdc9457SAndroid Build Coastguard Worker$SIMD_TILE = BATCH_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$if AVX: 13*4bdc9457SAndroid Build Coastguard Worker #include <immintrin.h> 14*4bdc9457SAndroid Build Coastguard Worker$else: 15*4bdc9457SAndroid Build Coastguard Worker #include <tmmintrin.h> 16*4bdc9457SAndroid Build Coastguard Worker 17*4bdc9457SAndroid Build Coastguard Worker#include <xnnpack/common.h> 18*4bdc9457SAndroid Build Coastguard Worker$if AVX: 19*4bdc9457SAndroid Build Coastguard Worker #include <xnnpack/intrinsics-polyfill.h> 20*4bdc9457SAndroid Build Coastguard Worker#include <xnnpack/lut.h> 21*4bdc9457SAndroid Build Coastguard Worker$if not AVX: 22*4bdc9457SAndroid Build Coastguard Worker #include <xnnpack/unaligned.h> 23*4bdc9457SAndroid Build Coastguard Worker 24*4bdc9457SAndroid Build Coastguard Worker 25*4bdc9457SAndroid Build Coastguard Workervoid xnn_x8_lut_ukernel__${"avx" if AVX else "ssse3"}_x${BATCH_TILE}( 26*4bdc9457SAndroid Build Coastguard Worker size_t n, 27*4bdc9457SAndroid Build Coastguard Worker const uint8_t* x, 28*4bdc9457SAndroid Build Coastguard Worker uint8_t* y, 29*4bdc9457SAndroid Build Coastguard Worker const uint8_t t[restrict XNN_MIN_ELEMENTS(256)]) 30*4bdc9457SAndroid Build Coastguard Worker{ 31*4bdc9457SAndroid Build Coastguard Worker assert(n != 0); 32*4bdc9457SAndroid Build Coastguard Worker assert(x != NULL); 33*4bdc9457SAndroid Build Coastguard Worker assert(y != NULL); 34*4bdc9457SAndroid Build Coastguard Worker 35*4bdc9457SAndroid Build Coastguard Worker const __m128i vt0 = _mm_load_si128((const __m128i*) t); 36*4bdc9457SAndroid Build Coastguard Worker $for T in range(1, 16): 37*4bdc9457SAndroid Build Coastguard Worker const __m128i vt${ABC[T]} = _mm_load_si128((const __m128i*) (t + ${T * 16})); 38*4bdc9457SAndroid Build Coastguard Worker 39*4bdc9457SAndroid Build Coastguard Worker const __m128i vtable0 = vt0; 40*4bdc9457SAndroid Build Coastguard Worker $for T in range(1, 8): 41*4bdc9457SAndroid Build Coastguard Worker const __m128i vtable${ABC[T]} = _mm_xor_si128(vt${ABC[T-1]}, vt${ABC[T]}); 42*4bdc9457SAndroid Build Coastguard Worker $for T in range(8, 16): 43*4bdc9457SAndroid Build Coastguard Worker const __m128i vtable${ABC[T]} = _mm_xor_si128(_mm_xor_si128(vt${ABC[T-1]}, vt${ABC[T]}), vtable${ABC[T-8]}); 44*4bdc9457SAndroid Build Coastguard Worker 45*4bdc9457SAndroid Build Coastguard Worker const __m128i voffset = _mm_set1_epi8(16); 46*4bdc9457SAndroid Build Coastguard Worker $if BATCH_TILE > 16: 47*4bdc9457SAndroid Build Coastguard Worker for (; n >= ${BATCH_TILE} * sizeof(uint8_t); n -= ${BATCH_TILE} * sizeof(uint8_t)) { 48*4bdc9457SAndroid Build Coastguard Worker __m128i vx0 = _mm_loadu_si128((const __m128i*) x); 49*4bdc9457SAndroid Build Coastguard Worker $for N in range(1, SIMD_TILE): 50*4bdc9457SAndroid Build Coastguard Worker __m128i vx${N} = _mm_loadu_si128((const __m128i*) (x + ${N * 16})); 51*4bdc9457SAndroid Build Coastguard Worker x += ${BATCH_TILE}; 52*4bdc9457SAndroid Build Coastguard Worker 53*4bdc9457SAndroid Build Coastguard Worker $for N in range(SIMD_TILE): 54*4bdc9457SAndroid Build Coastguard Worker __m128i vy${N} = _mm_shuffle_epi8(vtable0, vx${N}); 55*4bdc9457SAndroid Build Coastguard Worker 56*4bdc9457SAndroid Build Coastguard Worker $for T in range(1, 9): 57*4bdc9457SAndroid Build Coastguard Worker $for N in range(SIMD_TILE): 58*4bdc9457SAndroid Build Coastguard Worker vx${N} = _mm_sub_epi8(vx${N}, voffset); 59*4bdc9457SAndroid Build Coastguard Worker $for N in range(SIMD_TILE): 60*4bdc9457SAndroid Build Coastguard Worker vy${N} = _mm_xor_si128(vy${N}, _mm_shuffle_epi8(vtable${ABC[T]}, vx${N})); 61*4bdc9457SAndroid Build Coastguard Worker 62*4bdc9457SAndroid Build Coastguard Worker $for T in range(9, 16): 63*4bdc9457SAndroid Build Coastguard Worker $for N in range(SIMD_TILE): 64*4bdc9457SAndroid Build Coastguard Worker vx${N} = _mm_subs_epi8(vx${N}, voffset); 65*4bdc9457SAndroid Build Coastguard Worker $for N in range(SIMD_TILE): 66*4bdc9457SAndroid Build Coastguard Worker vy${N} = _mm_xor_si128(vy${N}, _mm_shuffle_epi8(vtable${ABC[T]}, vx${N})); 67*4bdc9457SAndroid Build Coastguard Worker 68*4bdc9457SAndroid Build Coastguard Worker _mm_storeu_si128((__m128i*) y, vy0); 69*4bdc9457SAndroid Build Coastguard Worker $for N in range(1, SIMD_TILE): 70*4bdc9457SAndroid Build Coastguard Worker _mm_storeu_si128((__m128i*) (y + ${N * 16}), vy${N}); 71*4bdc9457SAndroid Build Coastguard Worker y += ${BATCH_TILE}; 72*4bdc9457SAndroid Build Coastguard Worker } 73*4bdc9457SAndroid Build Coastguard Worker for (; n >= 16 * sizeof(uint8_t); n -= 16 * sizeof(uint8_t)) { 74*4bdc9457SAndroid Build Coastguard Worker __m128i vx = _mm_loadu_si128((const __m128i*) x); 75*4bdc9457SAndroid Build Coastguard Worker x += 16; 76*4bdc9457SAndroid Build Coastguard Worker 77*4bdc9457SAndroid Build Coastguard Worker __m128i vy = _mm_shuffle_epi8(vtable0, vx); 78*4bdc9457SAndroid Build Coastguard Worker 79*4bdc9457SAndroid Build Coastguard Worker $for T in range(1, 9): 80*4bdc9457SAndroid Build Coastguard Worker vx = _mm_sub_epi8(vx, voffset); 81*4bdc9457SAndroid Build Coastguard Worker vy = _mm_xor_si128(vy, _mm_shuffle_epi8(vtable${ABC[T]}, vx)); 82*4bdc9457SAndroid Build Coastguard Worker 83*4bdc9457SAndroid Build Coastguard Worker $for T in range(9, 16): 84*4bdc9457SAndroid Build Coastguard Worker vx = _mm_subs_epi8(vx, voffset); 85*4bdc9457SAndroid Build Coastguard Worker vy = _mm_xor_si128(vy, _mm_shuffle_epi8(vtable${ABC[T]}, vx)); 86*4bdc9457SAndroid Build Coastguard Worker 87*4bdc9457SAndroid Build Coastguard Worker _mm_storeu_si128((__m128i*) y, vy); 88*4bdc9457SAndroid Build Coastguard Worker y += 16; 89*4bdc9457SAndroid Build Coastguard Worker } 90*4bdc9457SAndroid Build Coastguard Worker if XNN_UNLIKELY(n != 0) { 91*4bdc9457SAndroid Build Coastguard Worker __m128i vx = _mm_loadu_si128((const __m128i*) x); 92*4bdc9457SAndroid Build Coastguard Worker 93*4bdc9457SAndroid Build Coastguard Worker __m128i vy = _mm_shuffle_epi8(vtable0, vx); 94*4bdc9457SAndroid Build Coastguard Worker 95*4bdc9457SAndroid Build Coastguard Worker $for T in range(1, 9): 96*4bdc9457SAndroid Build Coastguard Worker vx = _mm_sub_epi8(vx, voffset); 97*4bdc9457SAndroid Build Coastguard Worker vy = _mm_xor_si128(vy, _mm_shuffle_epi8(vtable${ABC[T]}, vx)); 98*4bdc9457SAndroid Build Coastguard Worker 99*4bdc9457SAndroid Build Coastguard Worker $for T in range(9, 16): 100*4bdc9457SAndroid Build Coastguard Worker vx = _mm_subs_epi8(vx, voffset); 101*4bdc9457SAndroid Build Coastguard Worker vy = _mm_xor_si128(vy, _mm_shuffle_epi8(vtable${ABC[T]}, vx)); 102*4bdc9457SAndroid Build Coastguard Worker 103*4bdc9457SAndroid Build Coastguard Worker if (n & (8 * sizeof(uint8_t))) { 104*4bdc9457SAndroid Build Coastguard Worker _mm_storel_epi64((__m128i*) y, vy); 105*4bdc9457SAndroid Build Coastguard Worker vy = _mm_unpackhi_epi64(vy, vy); 106*4bdc9457SAndroid Build Coastguard Worker y += 8; 107*4bdc9457SAndroid Build Coastguard Worker } 108*4bdc9457SAndroid Build Coastguard Worker if (n & (4 * sizeof(uint8_t))) { 109*4bdc9457SAndroid Build Coastguard Worker $if AVX: 110*4bdc9457SAndroid Build Coastguard Worker _mm_storeu_si32(y, vy); 111*4bdc9457SAndroid Build Coastguard Worker $else: 112*4bdc9457SAndroid Build Coastguard Worker unaligned_store_u32(y, (uint32_t) _mm_cvtsi128_si32(vy)); 113*4bdc9457SAndroid Build Coastguard Worker vy = _mm_srli_epi64(vy, 32); 114*4bdc9457SAndroid Build Coastguard Worker y += 4; 115*4bdc9457SAndroid Build Coastguard Worker } 116*4bdc9457SAndroid Build Coastguard Worker $if AVX: 117*4bdc9457SAndroid Build Coastguard Worker if (n & (2 * sizeof(uint8_t))) { 118*4bdc9457SAndroid Build Coastguard Worker _mm_storeu_si16(y, vy); 119*4bdc9457SAndroid Build Coastguard Worker vy = _mm_srli_epi32(vy, 16); 120*4bdc9457SAndroid Build Coastguard Worker y += 2; 121*4bdc9457SAndroid Build Coastguard Worker } 122*4bdc9457SAndroid Build Coastguard Worker if (n & (1 * sizeof(uint8_t))) { 123*4bdc9457SAndroid Build Coastguard Worker *y = (uint8_t) _mm_extract_epi8(vy, 0); 124*4bdc9457SAndroid Build Coastguard Worker } 125*4bdc9457SAndroid Build Coastguard Worker $else: 126*4bdc9457SAndroid Build Coastguard Worker uint32_t vy_lo = (uint32_t) _mm_cvtsi128_si32(vy); 127*4bdc9457SAndroid Build Coastguard Worker if (n & (2 * sizeof(uint8_t))) { 128*4bdc9457SAndroid Build Coastguard Worker unaligned_store_u16(y, (uint16_t) vy_lo); 129*4bdc9457SAndroid Build Coastguard Worker vy_lo >>= 16; 130*4bdc9457SAndroid Build Coastguard Worker y += 2; 131*4bdc9457SAndroid Build Coastguard Worker } 132*4bdc9457SAndroid Build Coastguard Worker if (n & (1 * sizeof(uint8_t))) { 133*4bdc9457SAndroid Build Coastguard Worker *y = (uint8_t) vy_lo; 134*4bdc9457SAndroid Build Coastguard Worker } 135*4bdc9457SAndroid Build Coastguard Worker } 136*4bdc9457SAndroid Build Coastguard Worker} 137