src/third_party/libvpx/vp9/common/arm/neon/vp9_highbd_iht4x4_add_neon.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);
  int64x2x2_t s[7], t[4];
  int32x4_t s7;

  s[0].val[0] = vmull_lane_s32(vget_low_s32(io[0]), vget_low_s32(sinpi), 0);
  s[0].val[1] = vmull_lane_s32(vget_high_s32(io[0]), vget_low_s32(sinpi), 0);
  s[1].val[0] = vmull_lane_s32(vget_low_s32(io[0]), vget_low_s32(sinpi), 1);
  s[1].val[1] = vmull_lane_s32(vget_high_s32(io[0]), vget_low_s32(sinpi), 1);
  s[2].val[0] = vmull_lane_s32(vget_low_s32(io[1]), vget_high_s32(sinpi), 0);
  s[2].val[1] = vmull_lane_s32(vget_high_s32(io[1]), vget_high_s32(sinpi), 0);
  s[3].val[0] = vmull_lane_s32(vget_low_s32(io[2]), vget_high_s32(sinpi), 1);
  s[3].val[1] = vmull_lane_s32(vget_high_s32(io[2]), vget_high_s32(sinpi), 1);
  s[4].val[0] = vmull_lane_s32(vget_low_s32(io[2]), vget_low_s32(sinpi), 0);
  s[4].val[1] = vmull_lane_s32(vget_high_s32(io[2]), vget_low_s32(sinpi), 0);
  s[5].val[0] = vmull_lane_s32(vget_low_s32(io[3]), vget_low_s32(sinpi), 1);
  s[5].val[1] = vmull_lane_s32(vget_high_s32(io[3]), vget_low_s32(sinpi), 1);
  s[6].val[0] = vmull_lane_s32(vget_low_s32(io[3]), vget_high_s32(sinpi), 1);
  s[6].val[1] = vmull_lane_s32(vget_high_s32(io[3]), vget_high_s32(sinpi), 1);
  s7 = vsubq_s32(io[0], io[2]);
  s7 = vaddq_s32(s7, io[3]);

  s[0].val[0] = vaddq_s64(s[0].val[0], s[3].val[0]);
  s[0].val[1] = vaddq_s64(s[0].val[1], s[3].val[1]);
  s[0].val[0] = vaddq_s64(s[0].val[0], s[5].val[0]);
  s[0].val[1] = vaddq_s64(s[0].val[1], s[5].val[1]);
  s[1].val[0] = vsubq_s64(s[1].val[0], s[4].val[0]);
  s[1].val[1] = vsubq_s64(s[1].val[1], s[4].val[1]);
  s[1].val[0] = vsubq_s64(s[1].val[0], s[6].val[0]);
  s[1].val[1] = vsubq_s64(s[1].val[1], s[6].val[1]);
  s[3] = s[2];
  s[2].val[0] = vmull_lane_s32(vget_low_s32(s7), vget_high_s32(sinpi), 0);
  s[2].val[1] = vmull_lane_s32(vget_high_s32(s7), vget_high_s32(sinpi), 0);

  t[0].val[0] = vaddq_s64(s[0].val[0], s[3].val[0]);
  t[0].val[1] = vaddq_s64(s[0].val[1], s[3].val[1]);
  t[1].val[0] = vaddq_s64(s[1].val[0], s[3].val[0]);
  t[1].val[1] = vaddq_s64(s[1].val[1], s[3].val[1]);
  t[2] = s[2];
  t[3].val[0] = vaddq_s64(s[0].val[0], s[1].val[0]);
  t[3].val[1] = vaddq_s64(s[0].val[1], s[1].val[1]);
  t[3].val[0] = vsubq_s64(t[3].val[0], s[3].val[0]);
  t[3].val[1] = vsubq_s64(t[3].val[1], s[3].val[1]);
  io[0] = vcombine_s32(vrshrn_n_s64(t[0].val[0], DCT_CONST_BITS),
                       vrshrn_n_s64(t[0].val[1], DCT_CONST_BITS));
  io[1] = vcombine_s32(vrshrn_n_s64(t[1].val[0], DCT_CONST_BITS),
                       vrshrn_n_s64(t[1].val[1], DCT_CONST_BITS));
  io[2] = vcombine_s32(vrshrn_n_s64(t[2].val[0], DCT_CONST_BITS),
                       vrshrn_n_s64(t[2].val[1], DCT_CONST_BITS));
  io[3] = vcombine_s32(vrshrn_n_s64(t[3].val[0], DCT_CONST_BITS),
                       vrshrn_n_s64(t[3].val[1], 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);
}