| OLD | NEW |
| (Empty) |
| 1 /* | |
| 2 * Copyright (c) 2014 The WebM project authors. All Rights Reserved. | |
| 3 * | |
| 4 * Use of this source code is governed by a BSD-style license | |
| 5 * that can be found in the LICENSE file in the root of the source | |
| 6 * tree. An additional intellectual property rights grant can be found | |
| 7 * in the file PATENTS. All contributing project authors may | |
| 8 * be found in the AUTHORS file in the root of the source tree. | |
| 9 */ | |
| 10 | |
| 11 #include <arm_neon.h> | |
| 12 | |
| 13 void idct_dequant_0_2x_neon( | |
| 14 int16_t *q, | |
| 15 int16_t dq, | |
| 16 unsigned char *dst, | |
| 17 int stride) { | |
| 18 unsigned char *dst0; | |
| 19 int i, a0, a1; | |
| 20 int16x8x2_t q2Add; | |
| 21 int32x2_t d2s32, d4s32; | |
| 22 uint8x8_t d2u8, d4u8; | |
| 23 uint16x8_t q1u16, q2u16; | |
| 24 | |
| 25 a0 = ((q[0] * dq) + 4) >> 3; | |
| 26 a1 = ((q[16] * dq) + 4) >> 3; | |
| 27 q[0] = q[16] = 0; | |
| 28 q2Add.val[0] = vdupq_n_s16((int16_t)a0); | |
| 29 q2Add.val[1] = vdupq_n_s16((int16_t)a1); | |
| 30 | |
| 31 for (i = 0; i < 2; i++, dst += 4) { | |
| 32 dst0 = dst; | |
| 33 d2s32 = vld1_lane_s32((const int32_t *)dst0, d2s32, 0); | |
| 34 dst0 += stride; | |
| 35 d2s32 = vld1_lane_s32((const int32_t *)dst0, d2s32, 1); | |
| 36 dst0 += stride; | |
| 37 d4s32 = vld1_lane_s32((const int32_t *)dst0, d4s32, 0); | |
| 38 dst0 += stride; | |
| 39 d4s32 = vld1_lane_s32((const int32_t *)dst0, d4s32, 1); | |
| 40 | |
| 41 q1u16 = vaddw_u8(vreinterpretq_u16_s16(q2Add.val[i]), | |
| 42 vreinterpret_u8_s32(d2s32)); | |
| 43 q2u16 = vaddw_u8(vreinterpretq_u16_s16(q2Add.val[i]), | |
| 44 vreinterpret_u8_s32(d4s32)); | |
| 45 | |
| 46 d2u8 = vqmovun_s16(vreinterpretq_s16_u16(q1u16)); | |
| 47 d4u8 = vqmovun_s16(vreinterpretq_s16_u16(q2u16)); | |
| 48 | |
| 49 d2s32 = vreinterpret_s32_u8(d2u8); | |
| 50 d4s32 = vreinterpret_s32_u8(d4u8); | |
| 51 | |
| 52 dst0 = dst; | |
| 53 vst1_lane_s32((int32_t *)dst0, d2s32, 0); | |
| 54 dst0 += stride; | |
| 55 vst1_lane_s32((int32_t *)dst0, d2s32, 1); | |
| 56 dst0 += stride; | |
| 57 vst1_lane_s32((int32_t *)dst0, d4s32, 0); | |
| 58 dst0 += stride; | |
| 59 vst1_lane_s32((int32_t *)dst0, d4s32, 1); | |
| 60 } | |
| 61 return; | |
| 62 } | |
| OLD | NEW |