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 % 8 == 0 7*4bdc9457SAndroid Build Coastguard Worker$assert BATCH_TILE >= 8 8*4bdc9457SAndroid Build Coastguard Worker$SIMD_TILE = BATCH_TILE // 8 9*4bdc9457SAndroid Build Coastguard Worker#include <assert.h> 10*4bdc9457SAndroid Build Coastguard Worker 11*4bdc9457SAndroid Build Coastguard Worker#include <arm_neon.h> 12*4bdc9457SAndroid Build Coastguard Worker 13*4bdc9457SAndroid Build Coastguard Worker#include <xnnpack/common.h> 14*4bdc9457SAndroid Build Coastguard Worker#include <xnnpack/vcvt.h> 15*4bdc9457SAndroid Build Coastguard Worker 16*4bdc9457SAndroid Build Coastguard Worker 17*4bdc9457SAndroid Build Coastguard Workervoid xnn_f16_f32_vcvt_ukernel__neonfp16_x${BATCH_TILE}( 18*4bdc9457SAndroid Build Coastguard Worker size_t n, 19*4bdc9457SAndroid Build Coastguard Worker const void* input, 20*4bdc9457SAndroid Build Coastguard Worker float* output, 21*4bdc9457SAndroid Build Coastguard Worker const union xnn_f16_f32_cvt_params params[restrict XNN_MIN_ELEMENTS(1)]) XNN_OOB_READS 22*4bdc9457SAndroid Build Coastguard Worker{ 23*4bdc9457SAndroid Build Coastguard Worker assert(n != 0); 24*4bdc9457SAndroid Build Coastguard Worker assert(n % sizeof(uint16_t) == 0); 25*4bdc9457SAndroid Build Coastguard Worker assert(input != NULL); 26*4bdc9457SAndroid Build Coastguard Worker assert(output != NULL); 27*4bdc9457SAndroid Build Coastguard Worker 28*4bdc9457SAndroid Build Coastguard Worker const uint16_t* i = (const uint16_t*) input; 29*4bdc9457SAndroid Build Coastguard Worker $if BATCH_TILE > 8: 30*4bdc9457SAndroid Build Coastguard Worker for (; n >= ${BATCH_TILE} * sizeof(uint16_t); n -= ${BATCH_TILE} * sizeof(uint16_t)) { 31*4bdc9457SAndroid Build Coastguard Worker $for N in range(SIMD_TILE): 32*4bdc9457SAndroid Build Coastguard Worker const float16x8_t vh${N} = vreinterpretq_f16_u16(vld1q_u16(i)); i += 8; 33*4bdc9457SAndroid Build Coastguard Worker 34*4bdc9457SAndroid Build Coastguard Worker $for N in range(SIMD_TILE): 35*4bdc9457SAndroid Build Coastguard Worker const float32x4_t vf${2*N} = vcvt_f32_f16(vget_low_f16(vh${N})); 36*4bdc9457SAndroid Build Coastguard Worker const float32x4_t vf${2*N+1} = vcvt_f32_f16(vget_high_f16(vh${N})); 37*4bdc9457SAndroid Build Coastguard Worker 38*4bdc9457SAndroid Build Coastguard Worker $for N in range(2*SIMD_TILE): 39*4bdc9457SAndroid Build Coastguard Worker vst1q_f32(output, vf${N}); output += 4; 40*4bdc9457SAndroid Build Coastguard Worker } 41*4bdc9457SAndroid Build Coastguard Worker for (; n >= 8 * sizeof(uint16_t); n -= 8 * sizeof(uint16_t)) { 42*4bdc9457SAndroid Build Coastguard Worker const float16x8_t vh = vreinterpretq_f16_u16(vld1q_u16(i)); i += 8; 43*4bdc9457SAndroid Build Coastguard Worker 44*4bdc9457SAndroid Build Coastguard Worker const float32x4_t vf_lo = vcvt_f32_f16(vget_low_f16(vh)); 45*4bdc9457SAndroid Build Coastguard Worker const float32x4_t vf_hi = vcvt_f32_f16(vget_high_f16(vh)); 46*4bdc9457SAndroid Build Coastguard Worker 47*4bdc9457SAndroid Build Coastguard Worker vst1q_f32(output, vf_lo); output += 4; 48*4bdc9457SAndroid Build Coastguard Worker vst1q_f32(output, vf_hi); output += 4; 49*4bdc9457SAndroid Build Coastguard Worker } 50*4bdc9457SAndroid Build Coastguard Worker if XNN_UNLIKELY(n != 0) { 51*4bdc9457SAndroid Build Coastguard Worker assert(n >= 1 * sizeof(uint16_t)); 52*4bdc9457SAndroid Build Coastguard Worker assert(n <= 7 * sizeof(uint16_t)); 53*4bdc9457SAndroid Build Coastguard Worker const float16x8_t vh = vreinterpretq_f16_u16(vld1q_u16(i)); i += 8; 54*4bdc9457SAndroid Build Coastguard Worker 55*4bdc9457SAndroid Build Coastguard Worker float32x4_t vf = vcvt_f32_f16(vget_low_f16(vh)); 56*4bdc9457SAndroid Build Coastguard Worker if (n & (4 * sizeof(uint16_t))) { 57*4bdc9457SAndroid Build Coastguard Worker vst1q_f32(output, vf); output += 4; 58*4bdc9457SAndroid Build Coastguard Worker vf = vcvt_f32_f16(vget_high_f16(vh)); 59*4bdc9457SAndroid Build Coastguard Worker } 60*4bdc9457SAndroid Build Coastguard Worker float32x2_t vf_lo = vget_low_f32(vf); 61*4bdc9457SAndroid Build Coastguard Worker if (n & (2 * sizeof(uint16_t))) { 62*4bdc9457SAndroid Build Coastguard Worker vst1_f32(output, vf_lo); output += 2; 63*4bdc9457SAndroid Build Coastguard Worker vf_lo = vget_high_f32(vf); 64*4bdc9457SAndroid Build Coastguard Worker } 65*4bdc9457SAndroid Build Coastguard Worker if (n & (1 * sizeof(uint16_t))) { 66*4bdc9457SAndroid Build Coastguard Worker vst1_lane_f32(output, vf_lo, 0); 67*4bdc9457SAndroid Build Coastguard Worker } 68*4bdc9457SAndroid Build Coastguard Worker } 69*4bdc9457SAndroid Build Coastguard Worker} 70