From mboxrd@z Thu Jan  1 00:00:00 1970
Return-Path: <dev-bounces@dpdk.org>
Received: from dpdk.org (dpdk.org [92.243.14.124])
	by inbox.dpdk.org (Postfix) with ESMTP id 0B458A04A3;
	Tue, 16 Jun 2020 07:18:57 +0200 (CEST)
Received: from [92.243.14.124] (localhost [127.0.0.1])
	by dpdk.org (Postfix) with ESMTP id 388AF1B203;
	Tue, 16 Jun 2020 07:18:56 +0200 (CEST)
Received: from EUR03-VE1-obe.outbound.protection.outlook.com
 (mail-eopbgr50080.outbound.protection.outlook.com [40.107.5.80])
 by dpdk.org (Postfix) with ESMTP id 31520199BC
 for <dev@dpdk.org>; Tue, 16 Jun 2020 07:18:54 +0200 (CEST)
DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=armh.onmicrosoft.com; 
 s=selector2-armh-onmicrosoft-com;
 h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck;
 bh=RbrHb3JdNTMTHTbZQbhPOJ8Oon4MRGZUBTii6GVloCw=;
 b=IS18VHJ+ChfbQS6M+Xrm2o5zhi7NYn6CluUnadkXTV+i1aFfX4kE7Cpt8xPInHuuvreUdJA57WuLXx/onw6vTuJTkSWWPL5VjFoYRbRyiIw6QMQ2EgU6oKNHJDdW1+VHsOLwQr3tpzMX8+5FB4+bgjd5ykQ/BflfQ0yotAWl+Xc=
Received: from AM6PR08CA0012.eurprd08.prod.outlook.com (2603:10a6:20b:b2::24)
 by DB7PR08MB3722.eurprd08.prod.outlook.com (2603:10a6:10:33::14) with
 Microsoft SMTP Server (version=TLS1_2,
 cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.3088.22; Tue, 16 Jun
 2020 05:18:52 +0000
Received: from AM5EUR03FT017.eop-EUR03.prod.protection.outlook.com
 (2603:10a6:20b:b2:cafe::a4) by AM6PR08CA0012.outlook.office365.com
 (2603:10a6:20b:b2::24) with Microsoft SMTP Server (version=TLS1_2,
 cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.3088.18 via Frontend
 Transport; Tue, 16 Jun 2020 05:18:51 +0000
X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 63.35.35.123)
 smtp.mailfrom=arm.com; dpdk.org; dkim=pass (signature was verified)
 header.d=armh.onmicrosoft.com;dpdk.org; dmarc=bestguesspass action=none
 header.from=arm.com;
Received-SPF: Pass (protection.outlook.com: domain of arm.com designates
 63.35.35.123 as permitted sender) receiver=protection.outlook.com;
 client-ip=63.35.35.123; helo=64aa7808-outbound-1.mta.getcheckrecipient.com;
Received: from 64aa7808-outbound-1.mta.getcheckrecipient.com (63.35.35.123) by
 AM5EUR03FT017.mail.protection.outlook.com (10.152.16.89) with
 Microsoft SMTP
 Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id
 15.20.3088.18 via Frontend Transport; Tue, 16 Jun 2020 05:18:51 +0000
Received: ("Tessian outbound c26a22531de7:v59");
 Tue, 16 Jun 2020 05:18:51 +0000
X-CR-MTA-TID: 64aa7808
Received: from e8528adfbaec.1
 by 64aa7808-outbound-1.mta.getcheckrecipient.com id
 E5C81EC3-5660-4051-80EC-1630CD480499.1; 
 Tue, 16 Jun 2020 05:18:46 +0000
Received: from EUR03-AM5-obe.outbound.protection.outlook.com
 by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id e8528adfbaec.1
 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384);
 Tue, 16 Jun 2020 05:18:46 +0000
ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none;
 b=Jq6W5a4Vr9KRM3NtdQ2WqZ2XdOdY9ROvQz8ZveS1o6mk8RnMSxR8WzkX3T03BWttyYQKnXP/Y/jHp1E0VIX85bwfe+6pamSDrHkl0zMKoDI0CxwzTYjnddLJnWEwDLnQFHg/+l8ZDm3ZlQRMhAaWuPcvz3kNI3Ljp34e/zCL6j+jwIHjP6TN0/QTHCkzh8vebw7zWXnzTFHG1JmaItvoU3YXwl/hwTtINo6mUHLszyaLgXOcnZPtsMvmooTdjaZvLcdSfVfaS4HSyAHcoNLjq1+4jlUkWCh8ov/gfE2EAbFFdsH9aKJcMiaBDnHNXfQm89lpooOspGkmOKPsnhLHig==
ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; 
 s=arcselector9901;
 h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck;
 bh=RbrHb3JdNTMTHTbZQbhPOJ8Oon4MRGZUBTii6GVloCw=;
 b=YpXuPvDB3nFC+aLfv712o1AoRlcFwSj9o4x0Hqzf9aiZxj3tztyZdbZlNVqIu4FZeR9hNNUrQbhPXkmaHPlSBd59Ar3Xvi1qi8iXKbFqPkMhmQmfH7JtHqZCmFpreYkESWZMC7/PH6HGmg9RiO029+1MDxOFgE6Kw4NCLTMIxTCSoB3mu3u/ohMWcO0SFAE7TnrBnz01ZVdPquCH7ozt0Wtu78FxKo0Ne/g6mWnuDCp+wd38ruK21RhQAPjj8+j7SjIQ4+ik+tF/CpH0RNDrQqdN9BdcTA+dZEJoRDlB5dqbcikp0pvun9W9XuCjPzWEK0rVxrakx+JffT91FigZxg==
ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass
 smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass
 header.d=arm.com; arc=none
DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=armh.onmicrosoft.com; 
 s=selector2-armh-onmicrosoft-com;
 h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck;
 bh=RbrHb3JdNTMTHTbZQbhPOJ8Oon4MRGZUBTii6GVloCw=;
 b=IS18VHJ+ChfbQS6M+Xrm2o5zhi7NYn6CluUnadkXTV+i1aFfX4kE7Cpt8xPInHuuvreUdJA57WuLXx/onw6vTuJTkSWWPL5VjFoYRbRyiIw6QMQ2EgU6oKNHJDdW1+VHsOLwQr3tpzMX8+5FB4+bgjd5ykQ/BflfQ0yotAWl+Xc=
Received: from HE1PR0801MB2025.eurprd08.prod.outlook.com (2603:10a6:3:50::14)
 by HE1PR0801MB2121.eurprd08.prod.outlook.com (2603:10a6:3:80::10)
 with Microsoft SMTP Server (version=TLS1_2,
 cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.3088.21; Tue, 16 Jun
 2020 05:18:45 +0000
Received: from HE1PR0801MB2025.eurprd08.prod.outlook.com
 ([fe80::646e:c258:7269:f4b2]) by HE1PR0801MB2025.eurprd08.prod.outlook.com
 ([fe80::646e:c258:7269:f4b2%11]) with mapi id 15.20.3088.029; Tue, 16 Jun
 2020 05:18:45 +0000
From: Ruifeng Wang <Ruifeng.Wang@arm.com>
To: Lance Richardson <lance.richardson@broadcom.com>, "dev@dpdk.org"
 <dev@dpdk.org>, "Ajit Khaparde (ajit.khaparde@broadcom.com)"
 <ajit.khaparde@broadcom.com>
Thread-Topic: [dpdk-dev] [PATCH 3/3] net/bnxt: add ARM64 vector support
Thread-Index: AQHWQExdbRod1Ejr60uxI/gdLyF2l6jakXiA
Date: Tue, 16 Jun 2020 05:18:44 +0000
Message-ID: <HE1PR0801MB20251519B4173FBFD8D2643F9E9D0@HE1PR0801MB2025.eurprd08.prod.outlook.com>
References: <20200611235817.208091-1-lance.richardson@broadcom.com>
 <20200611235817.208091-4-lance.richardson@broadcom.com>
In-Reply-To: <20200611235817.208091-4-lance.richardson@broadcom.com>
Accept-Language: en-US
Content-Language: en-US
X-MS-Has-Attach: 
X-MS-TNEF-Correlator: 
x-ts-tracking-id: 19322f07-d59a-44ec-8231-fac7eb7c0c68.0
x-checkrecipientchecked: true
Authentication-Results-Original: broadcom.com; dkim=none (message not signed)
 header.d=none; broadcom.com;
 dmarc=none action=none header.from=arm.com; 
x-originating-ip: [203.126.0.111]
x-ms-publictraffictype: Email
X-MS-Office365-Filtering-HT: Tenant
X-MS-Office365-Filtering-Correlation-Id: 92f7186d-6456-490b-66b9-08d811b4c1fa
x-ms-traffictypediagnostic: HE1PR0801MB2121:|DB7PR08MB3722:
x-ld-processed: f34e5979-57d9-4aaa-ad4d-b122a662184d,ExtAddr
X-Microsoft-Antispam-PRVS: <DB7PR08MB372271F18FF5A24BF46684F69E9D0@DB7PR08MB3722.eurprd08.prod.outlook.com>
x-checkrecipientrouted: true
nodisclaimer: true
x-ms-oob-tlc-oobclassifiers: OLM:179;OLM:7219;
x-forefront-prvs: 04362AC73B
X-MS-Exchange-SenderADCheck: 1
X-Microsoft-Antispam-Untrusted: BCL:0;
X-Microsoft-Antispam-Message-Info-Original: ZlvcdqZzYSUgr6lfoBn06Tf7uAFRsVPG/EC4j9dFuAB31MJRtArXvWzMjSP2z/RZBMjop1RM/E2UgXvcKvdjq4B/BL2CmuyZ2UkRcRcD4TRjX3xhlULaXls7jSc+yGz33csUKSJcwosM0hKb8Up3fXfZwg4Vq6nbQ+qEO1ADownu+rEJjZWvYqv89VPF9hEBfnV0UJHy026dCe0x5/azw19cnyKqruGk9/rCxGmSGnM746De1wgdFipt7a0JXEKm+tpbaowZh49nWGQWSQ7OEHjVOMVw66jHMnq6hZzBxsZa2oMtnqagLVKxNFJdCZ51
X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255; CTRY:; LANG:en;
 SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:HE1PR0801MB2025.eurprd08.prod.outlook.com;
 PTR:; CAT:NONE; SFTY:;
 SFS:(4636009)(39860400002)(136003)(396003)(346002)(366004)(376002)(83380400001)(5660300002)(8936002)(8676002)(71200400001)(316002)(52536014)(26005)(186003)(110136005)(7696005)(478600001)(53546011)(66476007)(66556008)(64756008)(66446008)(33656002)(6506007)(76116006)(66946007)(2906002)(86362001)(55016002)(9686003);
 DIR:OUT; SFP:1101; 
x-ms-exchange-antispam-messagedata: GOQHE5rzPukHw26O5yroFQ8bK7+8pNOYyuVcD4PRfDRUHLhUsSl9QGSq5pH27dHyEakaqCOCRDX3LDiFxHgwTxLMcAgE/gxViaXpcUHIQhTDfZkfA5Nad0+JKYAp7jRuz0n4dDzg196FNOpXfHkfL6E0BCpssQwWAu9gMABVS+oUH4dX597vP5lpSCX0H007uYxBDWCDRBE1J/Net0vslROn1VeqYiOeNPtxc6XQr1xKQBWatYksJxNlA0w2JmiIyecW8RNInq1QJPoAVINtYt7o3M9Kif/rqeeA0yw//vktTtmVZ0whfmEpQETGMMNw1uvBRqb5RB+Blg+4vm0zcLqNO2h4++zU24zWSe/RtrpPgTOF9kvahMJP2XknScSOVh/VJx9wDklx19iz6Zk/h7f1fgerUbCsrVNpEFpnTn4ghLJffKPWyREpZJIgCTfyovc7BaiBkK19/oURTmYzCSnkyyDVy4yMOi1BC51euYE=
x-ms-exchange-transport-forked: True
Content-Type: text/plain; charset="us-ascii"
Content-Transfer-Encoding: quoted-printable
MIME-Version: 1.0
X-MS-Exchange-Transport-CrossTenantHeadersStamped: HE1PR0801MB2121
Original-Authentication-Results: broadcom.com; dkim=none (message not signed)
 header.d=none; broadcom.com;
 dmarc=none action=none header.from=arm.com; 
X-EOPAttributedMessage: 0
X-MS-Exchange-Transport-CrossTenantHeadersStripped: AM5EUR03FT017.eop-EUR03.prod.protection.outlook.com
X-Forefront-Antispam-Report: CIP:63.35.35.123; CTRY:IE; LANG:en; SCL:1; SRV:;
 IPV:CAL; SFV:NSPM; H:64aa7808-outbound-1.mta.getcheckrecipient.com;
 PTR:ec2-63-35-35-123.eu-west-1.compute.amazonaws.com; CAT:NONE; SFTY:;
 SFS:(4636009)(136003)(396003)(346002)(376002)(39860400002)(46966005)(316002)(8936002)(8676002)(36906005)(110136005)(52536014)(5660300002)(55016002)(82740400003)(26005)(356005)(53546011)(6506007)(186003)(83380400001)(81166007)(7696005)(82310400002)(336012)(70206006)(33656002)(70586007)(47076004)(2906002)(9686003)(478600001)(86362001);
 DIR:OUT; SFP:1101; 
X-MS-Office365-Filtering-Correlation-Id-Prvs: b44b8d85-3f52-4566-c85a-08d811b4bddc
X-Forefront-PRVS: 04362AC73B
X-Microsoft-Antispam: BCL:0;
X-Microsoft-Antispam-Message-Info: pj31ViUGrXVCjcmuepUpTxPGG28+OZS9cQDAHJZhzJh+N8efGVJ3ojWI0r1oBxBZdxM8Zj3Dl5iZGrx8wtRpx9d/EaLikAzO7ULZ/Xltrfz8rCzPEADb52+flIWBk8MT3Q+sL0YH/OU0kQWnpBR19OcRnLV5kW/osnwcau1EKQ2iypopOgVgxcbvJDy85hkW3LB9m87CVCA/2st/+Xo9AdTJhuIY7aYsxvR2wbN0xmK2pnKqyhEYgRUri6Mu0W6TV3tre+NXk+xhoV+f12KDVf8HC5fAxGHp8XR9v6LKmxtALzXRc1OsMifog8EAQCIm9aI9M+9TNLNelyS0d+Kf50qr+ffXyvnXd+dNbZmbXlU/7xsL3FeR5dpJihUP6nY+50Xd3w+W65Np5nljgqjYvQ==
X-OriginatorOrg: arm.com
X-MS-Exchange-CrossTenant-OriginalArrivalTime: 16 Jun 2020 05:18:51.8569 (UTC)
X-MS-Exchange-CrossTenant-Network-Message-Id: 92f7186d-6456-490b-66b9-08d811b4c1fa
X-MS-Exchange-CrossTenant-Id: f34e5979-57d9-4aaa-ad4d-b122a662184d
X-MS-Exchange-CrossTenant-OriginalAttributedTenantConnectingIp: TenantId=f34e5979-57d9-4aaa-ad4d-b122a662184d; Ip=[63.35.35.123];
 Helo=[64aa7808-outbound-1.mta.getcheckrecipient.com]
X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem
X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB7PR08MB3722
Subject: Re: [dpdk-dev] [PATCH 3/3] net/bnxt: add ARM64 vector support
X-BeenThere: dev@dpdk.org
X-Mailman-Version: 2.1.15
Precedence: list
List-Id: DPDK patches and discussions <dev.dpdk.org>
List-Unsubscribe: <https://mails.dpdk.org/options/dev>,
 <mailto:dev-request@dpdk.org?subject=unsubscribe>
List-Archive: <http://mails.dpdk.org/archives/dev/>
List-Post: <mailto:dev@dpdk.org>
List-Help: <mailto:dev-request@dpdk.org?subject=help>
List-Subscribe: <https://mails.dpdk.org/listinfo/dev>,
 <mailto:dev-request@dpdk.org?subject=subscribe>
Errors-To: dev-bounces@dpdk.org
Sender: "dev" <dev-bounces@dpdk.org>


> -----Original Message-----
> From: dev <dev-bounces@dpdk.org> On Behalf Of Lance Richardson
> Sent: Friday, June 12, 2020 7:58 AM
> To: dev@dpdk.org; Ajit Khaparde (ajit.khaparde@broadcom.com)
> <ajit.khaparde@broadcom.com>
> Subject: [dpdk-dev] [PATCH 3/3] net/bnxt: add ARM64 vector support
>
> Add bnxt vector PMD support using NEON SIMD instructions.
>
> Signed-off-by: Lance Richardson <lance.richardson@broadcom.com>
> Reviewed-by: Ajit Kumar Khaparde <ajit.khaparde@broadcom.com>
> ---
>  drivers/net/bnxt/Makefile               |   3 +
>  drivers/net/bnxt/bnxt_ethdev.c          |  10 +-
>  drivers/net/bnxt/bnxt_ring.c            |   4 +-
>  drivers/net/bnxt/bnxt_rxq.h             |   2 +-
>  drivers/net/bnxt/bnxt_rxr.c             |   2 +-
>  drivers/net/bnxt/bnxt_rxr.h             |   2 +-
>  drivers/net/bnxt/bnxt_rxtx_vec_common.h |  57 +++
>  drivers/net/bnxt/bnxt_rxtx_vec_neon.c   | 473
> ++++++++++++++++++++++++
>  drivers/net/bnxt/bnxt_rxtx_vec_sse.c    |  46 +--
>  drivers/net/bnxt/bnxt_txr.h             |   2 +-
>  drivers/net/bnxt/meson.build            |   2 +
>  11 files changed, 548 insertions(+), 55 deletions(-)  create mode 100644
> drivers/net/bnxt/bnxt_rxtx_vec_common.h
>  create mode 100644 drivers/net/bnxt/bnxt_rxtx_vec_neon.c
>

<snip>

> diff --git a/drivers/net/bnxt/bnxt_rxtx_vec_neon.c
> b/drivers/net/bnxt/bnxt_rxtx_vec_neon.c
> new file mode 100644
> index 000000000..49620d03e
> --- /dev/null
> +++ b/drivers/net/bnxt/bnxt_rxtx_vec_neon.c
> @@ -0,0 +1,473 @@
> +/* SPDX-License-Identifier: BSD-3-Clause */
> +/* Copyright(c) 2019-2020 Broadcom All rights reserved. */
> +
> +#include <inttypes.h>
> +#include <stdbool.h>
> +
> +#include <rte_bitmap.h>
> +#include <rte_byteorder.h>
> +#include <rte_malloc.h>
> +#include <rte_memory.h>
> +#if defined(RTE_ARCH_ARM64)
> +#include <arm_neon.h>

rte_vect.h includes compatibility improvement. It can replace arm_neon.h he=
re.

> +#else
> +#error "bnxt vector pmd: unsupported target."
> +#endif
> +
> +#include "bnxt.h"
> +#include "bnxt_cpr.h"
> +#include "bnxt_ring.h"
> +#include "bnxt_rxr.h"
> +#include "bnxt_rxq.h"
> +#include "hsi_struct_def_dpdk.h"
> +#include "bnxt_rxtx_vec_common.h"
> +
> +#include "bnxt_txq.h"
> +#include "bnxt_txr.h"
> +

<snip>
IMPORTANT NOTICE: The contents of this email and any attachments are confid=
ential and may also be privileged. If you are not the intended recipient, p=
lease notify the sender immediately and do not disclose the contents to any=
 other person, use it for any purpose, or store or copy the information in =
any medium. Thank you.