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 64965A0350; Mon, 22 Jun 2020 03:29:32 +0200 (CEST) Received: from [92.243.14.124] (localhost [127.0.0.1]) by dpdk.org (Postfix) with ESMTP id C49E11C0D0; Mon, 22 Jun 2020 03:29:31 +0200 (CEST) Received: from EUR04-VI1-obe.outbound.protection.outlook.com (mail-eopbgr80043.outbound.protection.outlook.com [40.107.8.43]) by dpdk.org (Postfix) with ESMTP id D8E441C0C4 for ; Mon, 22 Jun 2020 03:29:29 +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=ZA0F4IkkE2I1477sltodDeLuqSiw5nDCs9mi0vubdfE=; b=90+nE/kJnbzRUb9ESg5Sozor7RMFonum5NFA0p2o0YN+EIst9Gw8QLhqIY8xtbndlK5bqK4JocC4Qj8LYVT1PhAJ5bicxRysUvuA9BBStHuV0y5L+yZb+fBmcDj/bBPRRZPSsBbflxGgMS9go5qm9yThQhDaZI+EVyokrx69pio= Received: from AM6P194CA0095.EURP194.PROD.OUTLOOK.COM (2603:10a6:209:8f::36) by DB8PR08MB5161.eurprd08.prod.outlook.com (2603:10a6:10:ea::16) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.3109.22; Mon, 22 Jun 2020 01:29:28 +0000 Received: from AM5EUR03FT011.eop-EUR03.prod.protection.outlook.com (2603:10a6:209:8f:cafe::a6) by AM6P194CA0095.outlook.office365.com (2603:10a6:209:8f::36) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.3109.22 via Frontend Transport; Mon, 22 Jun 2020 01:29:28 +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 AM5EUR03FT011.mail.protection.outlook.com (10.152.16.152) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.3109.22 via Frontend Transport; Mon, 22 Jun 2020 01:29:28 +0000 Received: ("Tessian outbound f44be76249db:v59"); Mon, 22 Jun 2020 01:29:28 +0000 X-CR-MTA-TID: 64aa7808 Received: from b7abb5ea8798.1 by 64aa7808-outbound-1.mta.getcheckrecipient.com id 4A00DDAA-2DB9-4636-AD21-582E4FFA85E0.1; Mon, 22 Jun 2020 01:29:23 +0000 Received: from EUR04-HE1-obe.outbound.protection.outlook.com by 64aa7808-outbound-1.mta.getcheckrecipient.com with ESMTPS id b7abb5ea8798.1 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384); Mon, 22 Jun 2020 01:29:23 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=THgTuHmgzOh+QjFtcUjURI6/FQB/o/C+yPv1nVeFcMJGy15e4kqu62v5JUU/v8LrF6qKRPGOh4QuBIxKkh79r9ySnnHl/RvU0Y+4H4N9iwh2m8OPqAicAB4Reg32Zlsmuw9oF8lwdEh8TAEkE9QhOyrTdDfIbhsmhqwT0LX6th8Yb09hZ8UFa4TNcshtt3ugtXmlPyhTKzeM8HSYJO1DlHL/RKrnbkNas+xQKsYh8sx3QnGGuHYgIDGBJK0WIT4sZi6He8A6u/1VdzBSM35cTS288jLptdasdGSIDtS2X+XHjHdeHWRKldHWXE0rCOPjnTr2mmKssOR504aJaxEHWQ== 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=ZA0F4IkkE2I1477sltodDeLuqSiw5nDCs9mi0vubdfE=; b=KH2xiJWu8fkKE0tZS+KrG4DcilF9z5yG+r2RPjdwIu2gi7q8dLPAD3X/IOtcv8XjGrn9SVRDWTxH5v3Gqps8Jm2lz9uohk2MzWjvx5KomLT4QC7Rd6nVsEvQIrH1saAefc6LdshLBhBSOLgYFN9E9lO3D6ab537mPH1TELLyXuIxYrOPKE+en39GUwkCIol1zHT3X0nQGbzxW96TOODHNnSx4RLEXL58F1mOKMgaRbzco89pyiM0CUPxvPN+VtCNZr/b6cxk/ZyuFsGpMz1tGpzBNTQdgGrzCutLUCC25lVL/DN0ULubtSCzDL+78bv5rCVOEZEZbGpavf18ps1W4A== 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=ZA0F4IkkE2I1477sltodDeLuqSiw5nDCs9mi0vubdfE=; b=90+nE/kJnbzRUb9ESg5Sozor7RMFonum5NFA0p2o0YN+EIst9Gw8QLhqIY8xtbndlK5bqK4JocC4Qj8LYVT1PhAJ5bicxRysUvuA9BBStHuV0y5L+yZb+fBmcDj/bBPRRZPSsBbflxGgMS9go5qm9yThQhDaZI+EVyokrx69pio= Received: from HE1PR0801MB2025.eurprd08.prod.outlook.com (2603:10a6:3:50::14) by HE1PR0801MB1995.eurprd08.prod.outlook.com (2603:10a6:3:52::21) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.3109.22; Mon, 22 Jun 2020 01:29:20 +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.3109.027; Mon, 22 Jun 2020 01:29:20 +0000 From: Ruifeng Wang To: Lance Richardson , "dev@dpdk.org" , "Ajit Khaparde (ajit.khaparde@broadcom.com)" CC: nd Thread-Topic: [PATCH 3/3] net/bnxt: add ARM64 vector support Thread-Index: AQHWRX3Rx6x6TtWAlEWx7P45bSrTbqjj3c1Q Date: Mon, 22 Jun 2020 01:29:19 +0000 Message-ID: References: <20200618143532.258537-1-lance.richardson@broadcom.com> <20200618143532.258537-4-lance.richardson@broadcom.com> In-Reply-To: <20200618143532.258537-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: 1c5279cb-8d3b-4501-8202-ccf21abeec1d.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.112] x-ms-publictraffictype: Email X-MS-Office365-Filtering-HT: Tenant X-MS-Office365-Filtering-Correlation-Id: 9e026168-05f6-46fc-9029-08d8164bb4ad x-ms-traffictypediagnostic: HE1PR0801MB1995:|DB8PR08MB5161: x-ld-processed: f34e5979-57d9-4aaa-ad4d-b122a662184d,ExtAddr X-Microsoft-Antispam-PRVS: x-checkrecipientrouted: true nodisclaimer: true x-ms-oob-tlc-oobclassifiers: OLM:1360;OLM:1360; x-forefront-prvs: 0442E569BC X-MS-Exchange-SenderADCheck: 1 X-Microsoft-Antispam-Untrusted: BCL:0; X-Microsoft-Antispam-Message-Info-Original: T8NnuyLMT8C+v/xpZkeA03q92vs8V3pAwss0vgW8Lzfwbi6CuUlu4RLfagdF8t8vjgiXIRQrwsXAnhCBa5awIK+byfp2akzvp2xMzhAaWH5fyJ8BayHHGw32IUc1uGCQ52aeoQBqIa3XwTQB+J20Ti4MxQheIAmX6w9VyKLWJkAyl6NbNst0mybcGKc0OR43FvPFXCTtfVIj17JGBU4HoRp8hrCSVU6seZCWNFCV7RnerU9Viul4Uz/3FKabq29IPxZoyVvp8HnKB1NJbOxixnQNlmQuVkcLALZGjYV9lhzxB/TfWT2uwZXDNWLdI8kTWwmukRKjDwOUyaq9onrXtQ== 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)(39850400004)(396003)(136003)(376002)(346002)(366004)(64756008)(6506007)(66446008)(53546011)(9686003)(52536014)(8936002)(26005)(5660300002)(55016002)(8676002)(2906002)(186003)(86362001)(76116006)(66946007)(66556008)(66476007)(71200400001)(4326008)(33656002)(83380400001)(7696005)(110136005)(316002)(478600001); DIR:OUT; SFP:1101; x-ms-exchange-antispam-messagedata: VJ1N7+7diOwByG7ahcRvYRhRr8NY0Wbkz7Tt6hl98VluWOfD7P8Bl+LFVEArff9pjDmFcmcdxh5qxsJJ1eldtwcUEncksHAVmGk4MOHbZCsglw7I6lzTPz6jwSt3vAKWLBiYlgiLydDxflEYXji2CYdkp4dnLAAX+aKoNIRe2IowPuxFU5gRgu3L8kHuSogpwIycFVCVorJiZneJqsHO4ZWSjADhzC8K+VhvV/Fy1Mx+H2qCKNyiYDp5y3svXIo4NugOZRP5tZwRKW9A6rDt35x66YUDyFPoLLgrRdN4FP0T6yy7vAGPobuhD/ImInmra50jSut9pAcqNfDG0OuqBuHd+ec/iGLv8NEBvWGS2q8tXi6i+y8GoNC0gC5f6hA24wmsn3ZjLh34myLzv5GeyaagwjNpez+GIHHM67xrHXzZIWi4hx/tjEf28gN/ej/dyNlf5O6c8uaqKSw5twpaIXQtMRcslcPtlIdZbBqXzNg= 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: HE1PR0801MB1995 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: AM5EUR03FT011.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)(396003)(39850400004)(136003)(376002)(346002)(46966005)(82740400003)(81166007)(5660300002)(8936002)(110136005)(47076004)(2906002)(8676002)(4326008)(70586007)(9686003)(55016002)(336012)(83380400001)(478600001)(82310400002)(186003)(33656002)(70206006)(86362001)(7696005)(36906005)(356005)(52536014)(26005)(53546011)(6506007)(316002); DIR:OUT; SFP:1101; X-MS-Office365-Filtering-Correlation-Id-Prvs: a3b499a7-a1c2-4cc8-2e63-08d8164bafd0 X-Forefront-PRVS: 0442E569BC X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: AYcx0Uef3YknQCPiAKKf/siH+gtFHMlZroILPI/FSp5+Om+R3zqmUid8AhuX0lydmCgdjm5Kwh9kwl7n5o95PG8vD1XgiKCyqJXMjvfQOCwSECV4VKSWCov6if2i4ctIhQff8WS//8wAvzP2bxvhCJqm8A1OFUb9njDC0LaBtW0mPQWi6XlIm5nmGHrOjnPw9QhiHnSqGf66UPTWGCUSsScNRUca0ueIp9kn2/jj04BLmYLqghsHZbypMU+8xaZKzsdj+CQ8deE7j+j1bNFtNhh1Eshfub12UK9ev2DS6CgSSCsvQfGWWipUOZWdjwLq3z1KAPoL0cmDTxM7i+88ddQV4gDjggA2Nv5AMyvqJhJ03ukUZqYF1YmKfx7noMNtHWoqVYgZrpJnIPcpcussVA== X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 22 Jun 2020 01:29:28.1987 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 9e026168-05f6-46fc-9029-08d8164bb4ad 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: DB8PR08MB5161 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" > -----Original Message----- > From: Lance Richardson > Sent: Thursday, June 18, 2020 10:36 PM > To: dev@dpdk.org; Ajit Khaparde (ajit.khaparde@broadcom.com) > ; Ruifeng Wang > Subject: [PATCH 3/3] net/bnxt: add ARM64 vector support >=20 > Add bnxt vector PMD support using NEON SIMD instructions. >=20 > Signed-off-by: Lance Richardson > Reviewed-by: Ajit Kumar Khaparde > --- > v2: > - Use rte_vect.h instead of including arm_neon.h directly in > bnxt_rxtx_vec_neon.c. >=20 > 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 | 469 > ++++++++++++++++++++++++ > 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, 544 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 >=20 Reviewed-by: Ruifeng Wang