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 #include <assert.h> 7*4bdc9457SAndroid Build Coastguard Worker #include <stddef.h> 8*4bdc9457SAndroid Build Coastguard Worker #include <stdint.h> 9*4bdc9457SAndroid Build Coastguard Worker 10*4bdc9457SAndroid Build Coastguard Worker #include <immintrin.h> 11*4bdc9457SAndroid Build Coastguard Worker 12*4bdc9457SAndroid Build Coastguard Worker #include <xnnpack/math-stubs.h> 13*4bdc9457SAndroid Build Coastguard Worker 14*4bdc9457SAndroid Build Coastguard Worker xnn_math_f16_f32_cvt__f16c(size_t n,const void * input,float * output)15*4bdc9457SAndroid Build Coastguard Workervoid xnn_math_f16_f32_cvt__f16c( 16*4bdc9457SAndroid Build Coastguard Worker size_t n, 17*4bdc9457SAndroid Build Coastguard Worker const void* input, 18*4bdc9457SAndroid Build Coastguard Worker float* output) 19*4bdc9457SAndroid Build Coastguard Worker { 20*4bdc9457SAndroid Build Coastguard Worker assert(n % (8 * sizeof(float)) == 0); 21*4bdc9457SAndroid Build Coastguard Worker 22*4bdc9457SAndroid Build Coastguard Worker const uint16_t* i = (const uint16_t*) input; 23*4bdc9457SAndroid Build Coastguard Worker for (; n != 0; n -= 8 * sizeof(float)) { 24*4bdc9457SAndroid Build Coastguard Worker const __m128i vx = _mm_loadu_si128((const __m128i*) i); 25*4bdc9457SAndroid Build Coastguard Worker i += 8; 26*4bdc9457SAndroid Build Coastguard Worker 27*4bdc9457SAndroid Build Coastguard Worker const __m256 vy = _mm256_cvtph_ps(vx); 28*4bdc9457SAndroid Build Coastguard Worker 29*4bdc9457SAndroid Build Coastguard Worker _mm256_storeu_ps(output, vy); 30*4bdc9457SAndroid Build Coastguard Worker output += 8; 31*4bdc9457SAndroid Build Coastguard Worker } 32*4bdc9457SAndroid Build Coastguard Worker } 33