/external/XNNPACK/src/qs8-dwconv/gen/ |
D | up16x25-minmax-rndnu-neon-mul16.c | 367 const int16x8_t vi19x89ABCDEF = vmovl_s8(vld1_s8(i19)); i19 += 8; in xnn_qs8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mul16() local 372 vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi19x89ABCDEF), vget_low_s16(vk19x89ABCDEF)); in xnn_qs8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mul16() 373 vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi19x89ABCDEF), vget_high_s16(vk19x89ABCDEF)); in xnn_qs8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mul16()
|
D | up16x25-minmax-fp32-neonv8-mul16.c | 366 const int16x8_t vi19x89ABCDEF = vmovl_s8(vld1_s8(i19)); i19 += 8; in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mul16() local 371 vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi19x89ABCDEF), vget_low_s16(vk19x89ABCDEF)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mul16() 372 vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi19x89ABCDEF), vget_high_s16(vk19x89ABCDEF)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mul16()
|
D | up16x25-minmax-fp32-neon-mul16.c | 366 const int16x8_t vi19x89ABCDEF = vmovl_s8(vld1_s8(i19)); i19 += 8; in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__neon_mul16() local 371 vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi19x89ABCDEF), vget_low_s16(vk19x89ABCDEF)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__neon_mul16() 372 vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi19x89ABCDEF), vget_high_s16(vk19x89ABCDEF)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__neon_mul16()
|
D | up16x25-minmax-fp32-wasmsimd-mul16-add16.c | 397 const v128_t vi19x89ABCDEF = wasm_i16x8_load8x8(i19 + 8); in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__wasmsimd_mul16_add16() local 402 vprod89ABCDEF = wasm_i16x8_add(vprod89ABCDEF, wasm_i16x8_mul(vi19x89ABCDEF, vk19x89ABCDEF)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__wasmsimd_mul16_add16()
|
D | up16x25-minmax-rndnu-neon-mla8-ld64.c | 364 const int8x8_t vi19x89ABCDEF = vld1_s8(i19); i19 += 8; in xnn_qs8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mla8_ld64() local 368 vprod89ABCDEF = vmlal_s8(vprod89ABCDEF, vi19x89ABCDEF, vk19x89ABCDEF); in xnn_qs8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mla8_ld64()
|
D | up16x25-minmax-fp32-avx2-mul32.c | 341 … const __m256i vi19x89ABCDEF = _mm256_cvtepi8_epi32(_mm_loadl_epi64((const __m128i*) (i19 + 8))); in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__avx2_mul32() local 346 … vacc89ABCDEF = _mm256_add_epi32(vacc89ABCDEF, _mm256_mullo_epi32(vi19x89ABCDEF, vk19x89ABCDEF)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up16x25__avx2_mul32()
|
/external/XNNPACK/src/qc8-dwconv/gen/ |
D | up16x25-minmax-fp32-neon-mul16.c | 365 const int16x8_t vi19x89ABCDEF = vmovl_s8(vld1_s8(i19)); i19 += 8; in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neon_mul16() local 370 vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi19x89ABCDEF), vget_low_s16(vk19x89ABCDEF)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neon_mul16() 371 vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi19x89ABCDEF), vget_high_s16(vk19x89ABCDEF)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neon_mul16()
|
D | up16x25-minmax-fp32-neonv8-mul16.c | 365 const int16x8_t vi19x89ABCDEF = vmovl_s8(vld1_s8(i19)); i19 += 8; in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mul16() local 370 vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi19x89ABCDEF), vget_low_s16(vk19x89ABCDEF)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mul16() 371 vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi19x89ABCDEF), vget_high_s16(vk19x89ABCDEF)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mul16()
|
D | up16x25-minmax-fp32-avx2-mul32.c | 341 … const __m256i vi19x89ABCDEF = _mm256_cvtepi8_epi32(_mm_loadl_epi64((const __m128i*) (i19 + 8))); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__avx2_mul32() local 346 … vacc89ABCDEF = _mm256_add_epi32(vacc89ABCDEF, _mm256_mullo_epi32(vi19x89ABCDEF, vk19x89ABCDEF)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__avx2_mul32()
|
D | up16x25-minmax-fp32-neon-mla8-ld64.c | 362 const int8x8_t vi19x89ABCDEF = vld1_s8(i19); i19 += 8; in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neon_mla8_ld64() local 366 vprod89ABCDEF = vmlal_s8(vprod89ABCDEF, vi19x89ABCDEF, vk19x89ABCDEF); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neon_mla8_ld64()
|
D | up16x25-minmax-fp32-neonv8-mla8-ld64.c | 362 const int8x8_t vi19x89ABCDEF = vld1_s8(i19); i19 += 8; in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mla8_ld64() local 366 vprod89ABCDEF = vmlal_s8(vprod89ABCDEF, vi19x89ABCDEF, vk19x89ABCDEF); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mla8_ld64()
|
D | up16x25-minmax-fp32-wasmsimd-mul16-add16.c | 397 const v128_t vi19x89ABCDEF = wasm_i16x8_load8x8(i19 + 8); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__wasmsimd_mul16_add16() local 402 vprod89ABCDEF = wasm_i16x8_add(vprod89ABCDEF, wasm_i16x8_mul(vi19x89ABCDEF, vk19x89ABCDEF)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__wasmsimd_mul16_add16()
|
D | up16x25-minmax-fp32-sse2-mul16-add16.c | 511 const __m128i vi19x89ABCDEF = _mm_loadl_epi64((const __m128i*) (i19 + 8)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__sse2_mul16_add16() local 517 … const __m128i vxi19x89ABCDEF = _mm_srai_epi16(_mm_unpacklo_epi8(vi19x89ABCDEF, vi19x89ABCDEF), 8); in xnn_qc8_dwconv_minmax_fp32_ukernel_up16x25__sse2_mul16_add16()
|
/external/XNNPACK/src/qu8-dwconv/gen/ |
D | up16x25-minmax-fp32-wasmsimd-mul16.c | 474 const v128_t vi19x89ABCDEF = wasm_u16x8_load8x8(i19 + 8); in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__wasmsimd_mul16() local 477 vsumx89ABCDEF = wasm_i16x8_add(vsumx89ABCDEF, vi19x89ABCDEF); in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__wasmsimd_mul16() 481 vprod89ABCDEF = wasm_i16x8_mul(vi19x89ABCDEF, vk19x89ABCDEF); in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__wasmsimd_mul16()
|
D | up16x25-minmax-fp32-neon-mul16.c | 367 const int16x8_t vi19x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i19))); i19 += 8; in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__neon_mul16() local 372 vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi19x89ABCDEF), vget_low_s16(vk19x89ABCDEF)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__neon_mul16() 373 vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi19x89ABCDEF), vget_high_s16(vk19x89ABCDEF)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__neon_mul16()
|
D | up16x25-minmax-fp32-neonv8-mul16.c | 367 const int16x8_t vi19x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i19))); i19 += 8; in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mul16() local 372 vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi19x89ABCDEF), vget_low_s16(vk19x89ABCDEF)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mul16() 373 vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi19x89ABCDEF), vget_high_s16(vk19x89ABCDEF)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__neonv8_mul16()
|
D | up16x25-minmax-rndnu-neon-mul16.c | 368 const int16x8_t vi19x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i19))); i19 += 8; in xnn_qu8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mul16() local 373 vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi19x89ABCDEF), vget_low_s16(vk19x89ABCDEF)); in xnn_qu8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mul16() 374 vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi19x89ABCDEF), vget_high_s16(vk19x89ABCDEF)); in xnn_qu8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mul16()
|
D | up16x25-minmax-rndnu-neon-mul8.c | 444 const uint8x8_t vi19x89ABCDEF = vld1_u8(i19); i19 += 8; in xnn_qu8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mul8() local 449 vprod89ABCDEF = vmull_u8(vi19x89ABCDEF, vk19x89ABCDEF); in xnn_qu8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mul8() 450 vsum89ABCDEF = vaddw_u8(vsum89ABCDEF, vi19x89ABCDEF); in xnn_qu8_dwconv_minmax_rndnu_ukernel_up16x25__neon_mul8()
|
D | up16x25-minmax-fp32-avx2-mul32.c | 342 … const __m256i vi19x89ABCDEF = _mm256_cvtepu8_epi32(_mm_loadl_epi64((const __m128i*) (i19 + 8))); in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__avx2_mul32() local 347 … vacc89ABCDEF = _mm256_add_epi32(vacc89ABCDEF, _mm256_mullo_epi32(vi19x89ABCDEF, vk19x89ABCDEF)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up16x25__avx2_mul32()
|
/external/XNNPACK/src/f32-dwconv/gen/ |
D | up16x25-minmax-avx.c | 341 const __m256 vi19x89ABCDEF = _mm256_loadu_ps(i19 + 8); in xnn_f32_dwconv_minmax_ukernel_up16x25__avx() local 347 vacc89ABCDEFp0 = _mm256_add_ps(vacc89ABCDEFp0, _mm256_mul_ps(vi19x89ABCDEF, vk19x89ABCDEF)); in xnn_f32_dwconv_minmax_ukernel_up16x25__avx()
|
D | up16x25-minmax-fma3-acc2.c | 341 const __m256 vi19x89ABCDEF = _mm256_loadu_ps(i19 + 8); in xnn_f32_dwconv_minmax_ukernel_up16x25__fma3_acc2() local 347 vacc89ABCDEFp1 = _mm256_fmadd_ps(vi19x89ABCDEF, vk19x89ABCDEF, vacc89ABCDEFp1); in xnn_f32_dwconv_minmax_ukernel_up16x25__fma3_acc2()
|
D | up16x25-minmax-fma3.c | 341 const __m256 vi19x89ABCDEF = _mm256_loadu_ps(i19 + 8); in xnn_f32_dwconv_minmax_ukernel_up16x25__fma3() local 347 vacc89ABCDEFp0 = _mm256_fmadd_ps(vi19x89ABCDEF, vk19x89ABCDEF, vacc89ABCDEFp0); in xnn_f32_dwconv_minmax_ukernel_up16x25__fma3()
|
D | up16x25-minmax-avx-acc2.c | 341 const __m256 vi19x89ABCDEF = _mm256_loadu_ps(i19 + 8); in xnn_f32_dwconv_minmax_ukernel_up16x25__avx_acc2() local 347 vacc89ABCDEFp1 = _mm256_add_ps(vacc89ABCDEFp1, _mm256_mul_ps(vi19x89ABCDEF, vk19x89ABCDEF)); in xnn_f32_dwconv_minmax_ukernel_up16x25__avx_acc2()
|
/external/XNNPACK/src/f16-dwconv/gen/ |
D | up16x25-minmax-neonfp16arith-acc2.c | 305 const float16x8_t vi19x89ABCDEF = vld1q_f16(i19); i19 += 8; in xnn_f16_dwconv_minmax_ukernel_up16x25__neonfp16arith_acc2() local 309 vacc89ABCDEFp1 = vfmaq_f16(vacc89ABCDEFp1, vi19x89ABCDEF, vk19x89ABCDEF); in xnn_f16_dwconv_minmax_ukernel_up16x25__neonfp16arith_acc2()
|
D | up16x25-minmax-neonfp16arith.c | 305 const float16x8_t vi19x89ABCDEF = vld1q_f16(i19); i19 += 8; in xnn_f16_dwconv_minmax_ukernel_up16x25__neonfp16arith() local 309 vacc89ABCDEFp0 = vfmaq_f16(vacc89ABCDEFp0, vi19x89ABCDEF, vk19x89ABCDEF); in xnn_f16_dwconv_minmax_ukernel_up16x25__neonfp16arith()
|