From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: 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 ; 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 To: Lance Richardson , "dev@dpdk.org" , "Ajit Khaparde (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: 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: 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 List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: dev-bounces@dpdk.org Sender: "dev" Archived-At: List-Archive: > -----Original Message----- > From: dev On Behalf Of Lance Richardson > Sent: Friday, June 12, 2020 7:58 AM > To: dev@dpdk.org; Ajit Khaparde (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 > Reviewed-by: Ajit Kumar Khaparde > --- > 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 > > 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 > +#include > + > +#include > +#include > +#include > +#include > +#if defined(RTE_ARCH_ARM64) > +#include 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" > + 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.