161 lines
4.8 KiB
C
161 lines
4.8 KiB
C
/*
|
|
* Copyright (c) 2018 The WebM project authors. All Rights Reserved.
|
|
*
|
|
* Use of this source code is governed by a BSD-style license
|
|
* that can be found in the LICENSE file in the root of the source
|
|
* tree. An additional intellectual property rights grant can be found
|
|
* in the file PATENTS. All contributing project authors may
|
|
* be found in the AUTHORS file in the root of the source tree.
|
|
*/
|
|
|
|
#include <arm_neon.h>
|
|
#include <assert.h>
|
|
|
|
#include "./vp9_rtcd.h"
|
|
#include "./vpx_config.h"
|
|
#include "vp9/common/vp9_common.h"
|
|
#include "vp9/common/arm/neon/vp9_iht_neon.h"
|
|
#include "vpx_dsp/arm/highbd_idct_neon.h"
|
|
#include "vpx_dsp/arm/idct_neon.h"
|
|
#include "vpx_dsp/arm/mem_neon.h"
|
|
#include "vpx_dsp/txfm_common.h"
|
|
|
|
static INLINE void highbd_iadst4(int32x4_t *const io) {
|
|
const int32_t sinpis[4] = { sinpi_1_9, sinpi_2_9, sinpi_3_9, sinpi_4_9 };
|
|
const int32x4_t sinpi = vld1q_s32(sinpis);
|
|
int32x4_t s[8];
|
|
|
|
s[0] = vmulq_lane_s32(io[0], vget_low_s32(sinpi), 0);
|
|
s[1] = vmulq_lane_s32(io[0], vget_low_s32(sinpi), 1);
|
|
s[2] = vmulq_lane_s32(io[1], vget_high_s32(sinpi), 0);
|
|
s[3] = vmulq_lane_s32(io[2], vget_high_s32(sinpi), 1);
|
|
s[4] = vmulq_lane_s32(io[2], vget_low_s32(sinpi), 0);
|
|
s[5] = vmulq_lane_s32(io[3], vget_low_s32(sinpi), 1);
|
|
s[6] = vmulq_lane_s32(io[3], vget_high_s32(sinpi), 1);
|
|
s[7] = vsubq_s32(io[0], io[2]);
|
|
s[7] = vaddq_s32(s[7], io[3]);
|
|
|
|
s[0] = vaddq_s32(s[0], s[3]);
|
|
s[0] = vaddq_s32(s[0], s[5]);
|
|
s[1] = vsubq_s32(s[1], s[4]);
|
|
s[1] = vsubq_s32(s[1], s[6]);
|
|
s[3] = s[2];
|
|
s[2] = vmulq_lane_s32(s[7], vget_high_s32(sinpi), 0);
|
|
|
|
io[0] = vaddq_s32(s[0], s[3]);
|
|
io[1] = vaddq_s32(s[1], s[3]);
|
|
io[2] = s[2];
|
|
io[3] = vaddq_s32(s[0], s[1]);
|
|
io[3] = vsubq_s32(io[3], s[3]);
|
|
io[0] = vrshrq_n_s32(io[0], DCT_CONST_BITS);
|
|
io[1] = vrshrq_n_s32(io[1], DCT_CONST_BITS);
|
|
io[2] = vrshrq_n_s32(io[2], DCT_CONST_BITS);
|
|
io[3] = vrshrq_n_s32(io[3], DCT_CONST_BITS);
|
|
}
|
|
|
|
void vp9_highbd_iht4x4_16_add_neon(const tran_low_t *input, uint16_t *dest,
|
|
int stride, int tx_type, int bd) {
|
|
const int16x8_t max = vdupq_n_s16((1 << bd) - 1);
|
|
int16x8_t a[2];
|
|
int32x4_t c[4];
|
|
|
|
c[0] = vld1q_s32(input);
|
|
c[1] = vld1q_s32(input + 4);
|
|
c[2] = vld1q_s32(input + 8);
|
|
c[3] = vld1q_s32(input + 12);
|
|
|
|
if (bd == 8) {
|
|
a[0] = vcombine_s16(vmovn_s32(c[0]), vmovn_s32(c[1]));
|
|
a[1] = vcombine_s16(vmovn_s32(c[2]), vmovn_s32(c[3]));
|
|
transpose_s16_4x4q(&a[0], &a[1]);
|
|
|
|
switch (tx_type) {
|
|
case DCT_DCT:
|
|
idct4x4_16_kernel_bd8(a);
|
|
a[1] = vcombine_s16(vget_high_s16(a[1]), vget_low_s16(a[1]));
|
|
transpose_s16_4x4q(&a[0], &a[1]);
|
|
idct4x4_16_kernel_bd8(a);
|
|
a[1] = vcombine_s16(vget_high_s16(a[1]), vget_low_s16(a[1]));
|
|
break;
|
|
|
|
case ADST_DCT:
|
|
idct4x4_16_kernel_bd8(a);
|
|
a[1] = vcombine_s16(vget_high_s16(a[1]), vget_low_s16(a[1]));
|
|
transpose_s16_4x4q(&a[0], &a[1]);
|
|
iadst4(a);
|
|
break;
|
|
|
|
case DCT_ADST:
|
|
iadst4(a);
|
|
transpose_s16_4x4q(&a[0], &a[1]);
|
|
idct4x4_16_kernel_bd8(a);
|
|
a[1] = vcombine_s16(vget_high_s16(a[1]), vget_low_s16(a[1]));
|
|
break;
|
|
|
|
default:
|
|
assert(tx_type == ADST_ADST);
|
|
iadst4(a);
|
|
transpose_s16_4x4q(&a[0], &a[1]);
|
|
iadst4(a);
|
|
break;
|
|
}
|
|
a[0] = vrshrq_n_s16(a[0], 4);
|
|
a[1] = vrshrq_n_s16(a[1], 4);
|
|
} else {
|
|
switch (tx_type) {
|
|
case DCT_DCT: {
|
|
const int32x4_t cospis = vld1q_s32(kCospi32);
|
|
|
|
if (bd == 10) {
|
|
idct4x4_16_kernel_bd10(cospis, c);
|
|
idct4x4_16_kernel_bd10(cospis, c);
|
|
} else {
|
|
idct4x4_16_kernel_bd12(cospis, c);
|
|
idct4x4_16_kernel_bd12(cospis, c);
|
|
}
|
|
break;
|
|
}
|
|
|
|
case ADST_DCT: {
|
|
const int32x4_t cospis = vld1q_s32(kCospi32);
|
|
|
|
if (bd == 10) {
|
|
idct4x4_16_kernel_bd10(cospis, c);
|
|
} else {
|
|
idct4x4_16_kernel_bd12(cospis, c);
|
|
}
|
|
transpose_s32_4x4(&c[0], &c[1], &c[2], &c[3]);
|
|
highbd_iadst4(c);
|
|
break;
|
|
}
|
|
|
|
case DCT_ADST: {
|
|
const int32x4_t cospis = vld1q_s32(kCospi32);
|
|
|
|
transpose_s32_4x4(&c[0], &c[1], &c[2], &c[3]);
|
|
highbd_iadst4(c);
|
|
if (bd == 10) {
|
|
idct4x4_16_kernel_bd10(cospis, c);
|
|
} else {
|
|
idct4x4_16_kernel_bd12(cospis, c);
|
|
}
|
|
break;
|
|
}
|
|
|
|
default: {
|
|
assert(tx_type == ADST_ADST);
|
|
transpose_s32_4x4(&c[0], &c[1], &c[2], &c[3]);
|
|
highbd_iadst4(c);
|
|
transpose_s32_4x4(&c[0], &c[1], &c[2], &c[3]);
|
|
highbd_iadst4(c);
|
|
break;
|
|
}
|
|
}
|
|
a[0] = vcombine_s16(vqrshrn_n_s32(c[0], 4), vqrshrn_n_s32(c[1], 4));
|
|
a[1] = vcombine_s16(vqrshrn_n_s32(c[2], 4), vqrshrn_n_s32(c[3], 4));
|
|
}
|
|
|
|
highbd_idct4x4_1_add_kernel1(&dest, stride, a[0], max);
|
|
highbd_idct4x4_1_add_kernel1(&dest, stride, a[1], max);
|
|
}
|