1b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian/* 2b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian * Copyright (c) 2014 The WebM project authors. All Rights Reserved. 3b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian * 4b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian * Use of this source code is governed by a BSD-style license 5b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian * that can be found in the LICENSE file in the root of the source 6b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian * tree. An additional intellectual property rights grant can be found 7b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian * in the file PATENTS. All contributing project authors may 8b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian * be found in the AUTHORS file in the root of the source tree. 9b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian */ 10b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian 11b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian#include <arm_neon.h> 12b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian 13b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanianvoid vp8_dc_only_idct_add_neon( 14b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian int16_t input_dc, 15b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian unsigned char *pred_ptr, 16b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian int pred_stride, 17b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian unsigned char *dst_ptr, 18b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian int dst_stride) { 19b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian int i; 20b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian uint16_t a1 = ((input_dc + 4) >> 3); 21b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian uint32x2_t d2u32 = vdup_n_u32(0); 22b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian uint8x8_t d2u8; 23b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian uint16x8_t q1u16; 24b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian uint16x8_t qAdd; 25b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian 26b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian qAdd = vdupq_n_u16(a1); 27b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian 28b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian for (i = 0; i < 2; i++) { 29b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian d2u32 = vld1_lane_u32((const uint32_t *)pred_ptr, d2u32, 0); 30b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian pred_ptr += pred_stride; 31b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian d2u32 = vld1_lane_u32((const uint32_t *)pred_ptr, d2u32, 1); 32b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian pred_ptr += pred_stride; 33b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian 34b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian q1u16 = vaddw_u8(qAdd, vreinterpret_u8_u32(d2u32)); 35b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian d2u8 = vqmovun_s16(vreinterpretq_s16_u16(q1u16)); 36b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian 37b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian vst1_lane_u32((uint32_t *)dst_ptr, vreinterpret_u32_u8(d2u8), 0); 38b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian dst_ptr += dst_stride; 39b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian vst1_lane_u32((uint32_t *)dst_ptr, vreinterpret_u32_u8(d2u8), 1); 40b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian dst_ptr += dst_stride; 41b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian } 42b08e2e23eec181e9951df33cd704ac294c5407b6Vignesh Venkatasubramanian} 43