/external/XNNPACK/src/f16-dwconv/gen/ |
D | up32x25-minmax-neonfp16arith-acc2.c | 475 const float16x8_t vi23xOPQRSTUV = vld1q_f16(i23); i23 += 8; in xnn_f16_dwconv_minmax_ukernel_up32x25__neonfp16arith_acc2() local 483 vaccOPQRSTUVp1 = vfmaq_f16(vaccOPQRSTUVp1, vi23xOPQRSTUV, vk23xOPQRSTUV); in xnn_f16_dwconv_minmax_ukernel_up32x25__neonfp16arith_acc2()
|
D | up32x25-minmax-neonfp16arith.c | 475 const float16x8_t vi23xOPQRSTUV = vld1q_f16(i23); i23 += 8; in xnn_f16_dwconv_minmax_ukernel_up32x25__neonfp16arith() local 483 vaccOPQRSTUVp0 = vfmaq_f16(vaccOPQRSTUVp0, vi23xOPQRSTUV, vk23xOPQRSTUV); in xnn_f16_dwconv_minmax_ukernel_up32x25__neonfp16arith()
|
D | up32x25-minmax-fma3.c | 522 const __m256 vi23xOPQRSTUV = _mm256_cvtph_ps(_mm_loadu_si128((const __m128i*) (i23 + 24))); in xnn_f16_dwconv_minmax_ukernel_up32x25__fma3() local 532 …vaccOPQRSTUVp0 = _mm256_cvtph_ps(_mm256_cvtps_ph(_mm256_fmadd_ps(vi23xOPQRSTUV, vk23xOPQRSTUV, vac… in xnn_f16_dwconv_minmax_ukernel_up32x25__fma3()
|
D | up32x25-minmax-fma3-acc2.c | 522 const __m256 vi23xOPQRSTUV = _mm256_cvtph_ps(_mm_loadu_si128((const __m128i*) (i23 + 24))); in xnn_f16_dwconv_minmax_ukernel_up32x25__fma3_acc2() local 532 …vaccOPQRSTUVp1 = _mm256_cvtph_ps(_mm256_cvtps_ph(_mm256_fmadd_ps(vi23xOPQRSTUV, vk23xOPQRSTUV, vac… in xnn_f16_dwconv_minmax_ukernel_up32x25__fma3_acc2()
|
/external/XNNPACK/src/qs8-dwconv/gen/ |
D | up32x25-minmax-rndnu-neon-mul16.c | 599 const int16x8_t vi23xOPQRSTUV = vmovl_s8(vld1_s8(i23)); i23 += 8; in xnn_qs8_dwconv_minmax_rndnu_ukernel_up32x25__neon_mul16() local 608 vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi23xOPQRSTUV), vget_low_s16(vk23xOPQRSTUV)); in xnn_qs8_dwconv_minmax_rndnu_ukernel_up32x25__neon_mul16() 609 vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi23xOPQRSTUV), vget_high_s16(vk23xOPQRSTUV)); in xnn_qs8_dwconv_minmax_rndnu_ukernel_up32x25__neon_mul16()
|
D | up32x25-minmax-fp32-neon-mul16.c | 598 const int16x8_t vi23xOPQRSTUV = vmovl_s8(vld1_s8(i23)); i23 += 8; in xnn_qs8_dwconv_minmax_fp32_ukernel_up32x25__neon_mul16() local 607 vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi23xOPQRSTUV), vget_low_s16(vk23xOPQRSTUV)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up32x25__neon_mul16() 608 vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi23xOPQRSTUV), vget_high_s16(vk23xOPQRSTUV)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up32x25__neon_mul16()
|
D | up32x25-minmax-fp32-neonv8-mul16.c | 598 const int16x8_t vi23xOPQRSTUV = vmovl_s8(vld1_s8(i23)); i23 += 8; in xnn_qs8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16() local 607 vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi23xOPQRSTUV), vget_low_s16(vk23xOPQRSTUV)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16() 608 vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi23xOPQRSTUV), vget_high_s16(vk23xOPQRSTUV)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16()
|
D | up32x25-minmax-fp32-avx2-mul32.c | 521 … const __m256i vi23xOPQRSTUV = _mm256_cvtepi8_epi32(_mm_loadl_epi64((const __m128i*) (i23 + 24))); in xnn_qs8_dwconv_minmax_fp32_ukernel_up32x25__avx2_mul32() local 528 … vaccOPQRSTUV = _mm256_add_epi32(vaccOPQRSTUV, _mm256_mullo_epi32(vi23xOPQRSTUV, vk23xOPQRSTUV)); in xnn_qs8_dwconv_minmax_fp32_ukernel_up32x25__avx2_mul32()
|
/external/XNNPACK/src/qc8-dwconv/gen/ |
D | up32x25-minmax-fp32-neonv8-mul16.c | 597 const int16x8_t vi23xOPQRSTUV = vmovl_s8(vld1_s8(i23)); i23 += 8; in xnn_qc8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16() local 606 vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi23xOPQRSTUV), vget_low_s16(vk23xOPQRSTUV)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16() 607 vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi23xOPQRSTUV), vget_high_s16(vk23xOPQRSTUV)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16()
|
D | up32x25-minmax-fp32-neon-mul16.c | 597 const int16x8_t vi23xOPQRSTUV = vmovl_s8(vld1_s8(i23)); i23 += 8; in xnn_qc8_dwconv_minmax_fp32_ukernel_up32x25__neon_mul16() local 606 vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi23xOPQRSTUV), vget_low_s16(vk23xOPQRSTUV)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up32x25__neon_mul16() 607 vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi23xOPQRSTUV), vget_high_s16(vk23xOPQRSTUV)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up32x25__neon_mul16()
|
D | up32x25-minmax-fp32-avx2-mul32.c | 521 … const __m256i vi23xOPQRSTUV = _mm256_cvtepi8_epi32(_mm_loadl_epi64((const __m128i*) (i23 + 24))); in xnn_qc8_dwconv_minmax_fp32_ukernel_up32x25__avx2_mul32() local 528 … vaccOPQRSTUV = _mm256_add_epi32(vaccOPQRSTUV, _mm256_mullo_epi32(vi23xOPQRSTUV, vk23xOPQRSTUV)); in xnn_qc8_dwconv_minmax_fp32_ukernel_up32x25__avx2_mul32()
|
/external/XNNPACK/src/qu8-dwconv/gen/ |
D | up32x25-minmax-fp32-neonv8-mul16.c | 599 const int16x8_t vi23xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i23))); i23 += 8; in xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16() local 608 vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi23xOPQRSTUV), vget_low_s16(vk23xOPQRSTUV)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16() 609 vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi23xOPQRSTUV), vget_high_s16(vk23xOPQRSTUV)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16()
|
D | up32x25-minmax-fp32-neon-mul16.c | 599 const int16x8_t vi23xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i23))); i23 += 8; in xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__neon_mul16() local 608 vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi23xOPQRSTUV), vget_low_s16(vk23xOPQRSTUV)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__neon_mul16() 609 vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi23xOPQRSTUV), vget_high_s16(vk23xOPQRSTUV)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__neon_mul16()
|
D | up32x25-minmax-rndnu-neon-mul16.c | 600 const int16x8_t vi23xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i23))); i23 += 8; in xnn_qu8_dwconv_minmax_rndnu_ukernel_up32x25__neon_mul16() local 609 vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi23xOPQRSTUV), vget_low_s16(vk23xOPQRSTUV)); in xnn_qu8_dwconv_minmax_rndnu_ukernel_up32x25__neon_mul16() 610 vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi23xOPQRSTUV), vget_high_s16(vk23xOPQRSTUV)); in xnn_qu8_dwconv_minmax_rndnu_ukernel_up32x25__neon_mul16()
|
D | up32x25-minmax-rndnu-neon-mul8.c | 782 const uint8x8_t vi23xOPQRSTUV = vld1_u8(i23); i23 += 8; in xnn_qu8_dwconv_minmax_rndnu_ukernel_up32x25__neon_mul8() local 791 vprodOPQRSTUV = vmull_u8(vi23xOPQRSTUV, vk23xOPQRSTUV); in xnn_qu8_dwconv_minmax_rndnu_ukernel_up32x25__neon_mul8() 792 vsumOPQRSTUV = vaddw_u8(vsumOPQRSTUV, vi23xOPQRSTUV); in xnn_qu8_dwconv_minmax_rndnu_ukernel_up32x25__neon_mul8()
|
D | up32x25-minmax-fp32-avx2-mul32.c | 522 … const __m256i vi23xOPQRSTUV = _mm256_cvtepu8_epi32(_mm_loadl_epi64((const __m128i*) (i23 + 24))); in xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__avx2_mul32() local 529 … vaccOPQRSTUV = _mm256_add_epi32(vaccOPQRSTUV, _mm256_mullo_epi32(vi23xOPQRSTUV, vk23xOPQRSTUV)); in xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__avx2_mul32()
|