From mboxrd@z Thu Jan  1 00:00:00 1970
Return-Path: <jianbo.liu@linaro.org>
Received: from mail-yw0-f173.google.com (mail-yw0-f173.google.com
 [209.85.161.173]) by dpdk.org (Postfix) with ESMTP id B6A1158CB
 for <dev@dpdk.org>; Mon, 10 Jul 2017 05:34:11 +0200 (CEST)
Received: by mail-yw0-f173.google.com with SMTP id l21so30624127ywb.1
 for <dev@dpdk.org>; Sun, 09 Jul 2017 20:34:11 -0700 (PDT)
DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=linaro.org; s=google;
 h=mime-version:in-reply-to:references:from:date:message-id:subject:to
 :cc; bh=brSwZtZWMCXa3op9Pkx4NQCc3GsMb+zCSfX7ifj6Y1c=;
 b=LddmxSXpfwXL9Q4hUxnCIwvcJ5MTlFtMGneBuF+GPpX78gOYX4KkWriFHp22coJGvV
 E1dyJgOZAJW6HFPzmKQ5KgnORkwuLp50j8nNe+s+vX0ZiE2dJuYsrDSTCdMJKRMIoxe+
 LPJzgKIIx3Nxu92wJnT84uVAZKuuY7m0NjUSw=
X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed;
 d=1e100.net; s=20161025;
 h=x-gm-message-state:mime-version:in-reply-to:references:from:date
 :message-id:subject:to:cc;
 bh=brSwZtZWMCXa3op9Pkx4NQCc3GsMb+zCSfX7ifj6Y1c=;
 b=UKVyeXY3bxNWDE8+xJBR2pMb7Gb5eqeoY5H3UhoBek+POhGsRPn/fS/qhG03p8TDXb
 j+4pT8sCdsipw8EAd3AecY8VNw2tN21TILYSXcWiz/lR95SPYmQ3n3mMfebfWMCSWasw
 ow2M7IMGCOptvVJSW/NUxCpWuof4Eonz/As/PELPhUkD7mMgGU+L88J+E0mFSpZ7ljdF
 NIulEDngUYWT9VKJwI7J+sbqwQRhRwpbtaaDnbmCLROjNrPiHuMAtflxN4jvWtwXS+8a
 abrlsVAoOaD0mV2l8hzFV2dhMkoFvZPdhvAQFCwTcck1MP/KA8cACM+MB46QFdty9WuV
 wsFw==
X-Gm-Message-State: AIVw111jrh5F+BF4wjT7ye5mlASXtZ7ANudnmkv0IxAXNGJlJv17+9o5
 EyzBiHJLESZrSTY1EAay+PVEwtFgFt6SmTxaIg==
X-Received: by 10.13.198.1 with SMTP id i1mr11223732ywd.288.1499657651089;
 Sun, 09 Jul 2017 20:34:11 -0700 (PDT)
MIME-Version: 1.0
Received: by 10.37.171.73 with HTTP; Sun, 9 Jul 2017 20:34:10 -0700 (PDT)
In-Reply-To: <20170707162654.4638-1-jerin.jacob@caviumnetworks.com>
References: <20170707162654.4638-1-jerin.jacob@caviumnetworks.com>
From: Jianbo Liu <jianbo.liu@linaro.org>
Date: Mon, 10 Jul 2017 11:34:10 +0800
Message-ID: <CAP4Qi38t-kR=b1nM4qRYOtoq9VP1-iB80K0hgB0Pv+L-8zq0qA@mail.gmail.com>
To: Jerin Jacob <jerin.jacob@caviumnetworks.com>
Cc: dev@dpdk.org, Thomas Monjalon <thomas@monjalon.net>, 
 Jan Viktorin <viktorin@rehivetech.com>
Content-Type: text/plain; charset="UTF-8"
Subject: Re: [dpdk-dev] [PATCH] eal/armv7: emulate vaddvq u16 variant
X-BeenThere: dev@dpdk.org
X-Mailman-Version: 2.1.15
Precedence: list
List-Id: DPDK patches and discussions <dev.dpdk.org>
List-Unsubscribe: <http://dpdk.org/ml/options/dev>,
 <mailto:dev-request@dpdk.org?subject=unsubscribe>
List-Archive: <http://dpdk.org/ml/archives/dev/>
List-Post: <mailto:dev@dpdk.org>
List-Help: <mailto:dev-request@dpdk.org?subject=help>
List-Subscribe: <http://dpdk.org/ml/listinfo/dev>,
 <mailto:dev-request@dpdk.org?subject=subscribe>
X-List-Received-Date: Mon, 10 Jul 2017 03:34:12 -0000

On 8 July 2017 at 00:26, Jerin Jacob <jerin.jacob@caviumnetworks.com> wrote:
> vaddvq_u16() is not available for armv7.
> Emulate the vaddvq_u16() using armv7 NEON intrinsics.
>
> Signed-off-by: Jerin Jacob <jerin.jacob@caviumnetworks.com>
> ---
>  lib/librte_eal/common/include/arch/arm/rte_vect.h | 11 +++++++++++
>  1 file changed, 11 insertions(+)
>
> diff --git a/lib/librte_eal/common/include/arch/arm/rte_vect.h b/lib/librte_eal/common/include/arch/arm/rte_vect.h
> index 0670ca2ee..69fd428f3 100644
> --- a/lib/librte_eal/common/include/arch/arm/rte_vect.h
> +++ b/lib/librte_eal/common/include/arch/arm/rte_vect.h
> @@ -77,6 +77,17 @@ vqtbl1q_u8(uint8x16_t a, uint8x16_t b)
>
>         return vld1q_u8(rte_ret.u8);
>  }
> +
> +static inline uint16_t
> +vaddvq_u16(uint16x8_t a)
> +{
> +       uint32x4_t m = vpaddlq_u16(a);
> +       uint64x2_t n = vpaddlq_u32(m);
> +       uint64x1_t o = vget_low_u64(n) + vget_high_u64(n);
> +
> +       return vget_lane_u32((uint32x2_t)o, 0);
> +}
> +
>  #endif
>
>  #if defined(RTE_TOOLCHAIN_GCC) && (GCC_VERSION < 70000)
> --
> 2.13.2
>

Acked-by: Jianbo Liu <jianbo.liu@linaro.org>