From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from mails.dpdk.org (mails.dpdk.org [217.70.189.124]) by inbox.dpdk.org (Postfix) with ESMTP id 6734841C8E; Tue, 14 Feb 2023 02:48:47 +0100 (CET) Received: from mails.dpdk.org (localhost [127.0.0.1]) by mails.dpdk.org (Postfix) with ESMTP id 4777240ED9; Tue, 14 Feb 2023 02:48:47 +0100 (CET) Received: from mga07.intel.com (mga07.intel.com [134.134.136.100]) by mails.dpdk.org (Postfix) with ESMTP id 08AB540E2D for ; Tue, 14 Feb 2023 02:48:44 +0100 (CET) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=intel.com; i=@intel.com; q=dns/txt; s=Intel; t=1676339325; x=1707875325; h=from:to:cc:subject:date:message-id:references: in-reply-to:content-transfer-encoding:mime-version; bh=SQLdSAw5WsYAtEQniKVXYQrKyeOECDfg9jTa0cuOcM0=; b=HG2ZFV4FM1RK/I2tgzKCDnw70LFR1/XbPwlrNbB8YuE0UsdgiMfSdTLV PPy/JTy2ZWRJMWKWCG30bFwXelpj20jHlK1OfrQcXbUKchI00OrNibaE5 kgMWeW2sVmeD46iaU+TV3zzLOun9NLdv5p1pcdMmHhLsIWf/oXr3msctu FdkAI2Y4HrcOygmUIPHcNHCgp2/gyWdsNBAl0HcNcTpa1F165MmWkIJkl ZwtyZpeR9S5csxq8G6DZXXmwwScv4hSfM3yVrwnwwa4+wxD0j7RKKdpuC luVIcmIkvpuJYrcFfILgjITk+zCsUYdf+zGrMDsCM6yZinkXGHjwo64WT w==; X-IronPort-AV: E=McAfee;i="6500,9779,10620"; a="395669299" X-IronPort-AV: E=Sophos;i="5.97,294,1669104000"; d="scan'208";a="395669299" Received: from orsmga002.jf.intel.com ([10.7.209.21]) by orsmga105.jf.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 13 Feb 2023 17:48:44 -0800 X-ExtLoop1: 1 X-IronPort-AV: E=McAfee;i="6500,9779,10620"; a="668999089" X-IronPort-AV: E=Sophos;i="5.97,294,1669104000"; d="scan'208";a="668999089" Received: from orsmsx601.amr.corp.intel.com ([10.22.229.14]) by orsmga002.jf.intel.com with ESMTP; 13 Feb 2023 17:48:43 -0800 Received: from orsmsx611.amr.corp.intel.com (10.22.229.24) by ORSMSX601.amr.corp.intel.com (10.22.229.14) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.16; Mon, 13 Feb 2023 17:48:42 -0800 Received: from orsmsx610.amr.corp.intel.com (10.22.229.23) by ORSMSX611.amr.corp.intel.com (10.22.229.24) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.16; Mon, 13 Feb 2023 17:48:42 -0800 Received: from ORSEDG602.ED.cps.intel.com (10.7.248.7) by orsmsx610.amr.corp.intel.com (10.22.229.23) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2507.16 via Frontend Transport; Mon, 13 Feb 2023 17:48:42 -0800 Received: from NAM11-CO1-obe.outbound.protection.outlook.com (104.47.56.174) by edgegateway.intel.com (134.134.137.103) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.1.2507.16; Mon, 13 Feb 2023 17:48:41 -0800 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=h17Lj8W5cD/2MID7/KWnNBo6HRmx8CPUA0rKvFWQ5MshCqmB1hYmbugxhl/uK3lMYX1xQdzhB8D9H78rX5khNduhs4ASDxJS0u30vXFTj6VsNfL0U5b/iUgCWZk0PzD2HXwXBIF65cLgJYP4VLHMP0894faPoGw8QwNzu17y4X8T5s+mAROcbb8l97zfLv7gpVsAnolVsB+l/fsZ228IE2S9aGArc/3AYydjp5qNaiLHfW075qGxpsrIbkHyflr+bnnTT5OQg15XHWTqfKcxMO2xMKmiNE8uEFP/eAEgAm6ry+IIa5VqWiVzT3p746as29xVXlNmuRqoEJ2pnj02Rw== 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-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=SQLdSAw5WsYAtEQniKVXYQrKyeOECDfg9jTa0cuOcM0=; b=Xgd8/XDjvJzmz6jmM8zHYPidE/wpBzoB1lHno8h30njjJnbkfPf1Z8zl3+jYQ17YCFH7BSSkdfyoqBYCX2G0z0eqfUQjOXNpvUOnF1iKM2CmZBeEzu7RJAAvyC5Bke+JR6UM//pbtLnZ0thVO4+E/ryVIQJI5Hz5e9wmRg2exxE4AyQaFbbC1mdg0IaiiWc6yX0FAEZG/aAvNyXd5ddRHdaC9X52GtJOMlnnx1LItn2jQE83VBj96kqnZA7oooKAC3ej1Jh9473viIGFBS2GEKfgJ5YgvAjbsJqUh8oGrj6bPaNQWngbyMEJr4YmLM/L7c6XzusEAAogXXCV0FE7Ag== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=intel.com; dmarc=pass action=none header.from=intel.com; dkim=pass header.d=intel.com; arc=none Received: from DM4PR11MB5994.namprd11.prod.outlook.com (2603:10b6:8:5d::20) by IA0PR11MB7695.namprd11.prod.outlook.com (2603:10b6:208:400::5) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.6086.24; Tue, 14 Feb 2023 01:48:38 +0000 Received: from DM4PR11MB5994.namprd11.prod.outlook.com ([fe80::eb70:80e0:1b88:3ca5]) by DM4PR11MB5994.namprd11.prod.outlook.com ([fe80::eb70:80e0:1b88:3ca5%9]) with mapi id 15.20.6086.024; Tue, 14 Feb 2023 01:48:38 +0000 From: "Zhang, Qi Z" To: "Lu, Wenzhuo" , mschmidt , "dev@dpdk.org" CC: "Richardson, Bruce" , "Wu, Jingjing" , "Xing, Beilei" , "Wang, Haiyue" Subject: RE: [PATCH] net/iavf: fix mbuf VLAN offload flags in the L2TAG2 path with AVX2 Thread-Topic: [PATCH] net/iavf: fix mbuf VLAN offload flags in the L2TAG2 path with AVX2 Thread-Index: AQHZCv9roM0yhPyq50epN7YTkO6U4a5sq06AgGFri+A= Date: Tue, 14 Feb 2023 01:48:38 +0000 Message-ID: References: <20221208121916.155132-1-mschmidt@redhat.com> In-Reply-To: Accept-Language: en-US Content-Language: en-US X-MS-Has-Attach: X-MS-TNEF-Correlator: authentication-results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=intel.com; x-ms-publictraffictype: Email x-ms-traffictypediagnostic: DM4PR11MB5994:EE_|IA0PR11MB7695:EE_ x-ms-office365-filtering-correlation-id: df99c455-cf9a-49bc-edfd-08db0e2d97da x-ld-processed: 46c98d88-e344-4ed4-8496-4ed7712e255d,ExtAddr x-ms-exchange-senderadcheck: 1 x-ms-exchange-antispam-relay: 0 x-microsoft-antispam: BCL:0; x-microsoft-antispam-message-info: eebPz7q4UGMihRQT8Q3mcjuLgodWWiV5aobenj4xtc17zU08c8CZCO9FTkLzdpz9Mx8+SdHA2pdWB4wGHM3Fl0I+KfTAz5+GAqja/WD7tfLpTo7fzv5lWCYQcd6RZlOfRFDNyIauNKGZNw6JSFau7cKpV3WueZn/vQMo5mdkYiLrGvGe+Tui9mZLbUG15lqx7CWLCjgu6oyzBlSW0vZzDcQLK66SdGc7/GlluG1xNo802lj1KFuW1UHWTHRkpXX+3EsaMlwzmWeDZHTw6aWuYIe+gE1HuEqbzxzia7Mpo1m96COlvq1QGy/oBlLXktvQc50UhSmQDL5yhvcKjJmmHocXEQr7BYFJ0zRElmbLQBRy/YDQFbA0M6wMMnqqJ/VwAzF6q+Mq947vFexg49vNYG7tRUjMJkhLRE5LvucykkRFyW7iQcHMrxjQmdDBy704KMDpUUbuRKOzKUCIq5lwGu2tVcDKG4PF6CYRBoQbBGUWQEPmn4tsSuMrWh9dLnlzu43pwYDenh1sXywCInnsk3D9C40FU5wkjopfTyQT97GABB9khTpjzj7tvh+pyYRLzogEXPS0RExms8ae2U4INxMuUMTXxpUqGzSmc9USFXOM2uiRlMeozjV6fppDhxJb377OWsIRiBtmAS9150qXyqRZtnjXBRDRC8DfhXlTAJoMu0jWba/rjEfbm9xeWB3kgVJv7HS68Shlg7CL/Lv57g== x-forefront-antispam-report: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:DM4PR11MB5994.namprd11.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230025)(396003)(136003)(346002)(376002)(366004)(39860400002)(451199018)(26005)(53546011)(186003)(9686003)(83380400001)(71200400001)(33656002)(6506007)(107886003)(4326008)(8936002)(5660300002)(52536014)(64756008)(8676002)(66476007)(66556008)(66946007)(76116006)(66446008)(2906002)(41300700001)(54906003)(55016003)(7696005)(110136005)(478600001)(316002)(82960400001)(38100700002)(122000001)(38070700005)(86362001); DIR:OUT; SFP:1102; x-ms-exchange-antispam-messagedata-chunkcount: 1 x-ms-exchange-antispam-messagedata-0: =?us-ascii?Q?0vu9G97j/xZMP2NHSnu6q9/JgYzRw7hEfOnIgHuFvwIiXxT6H30sNb48zlmx?= =?us-ascii?Q?PY1hTqtHaeBc5oHtoMd9KtumS2CHB3pbTP7kjCTDo8OPePxhqSrNhTlQwkzm?= =?us-ascii?Q?iqQUvIXJjfez6IdZEB+0fwYpZEP6LRoGnUX8F5xDXplyAC66As4MleYeHrwd?= =?us-ascii?Q?eQsI7H+Bbp5tT8sb8lF8XmCV+Z6ziIpZ4A9e0udlw5kRPBh1Zs6GJVAidSke?= =?us-ascii?Q?bvmeVuGb43ElXpRxgr3GkS9nT77tI6VwlGbz/FD5Zg/RVwDrhXldz91ycnZV?= =?us-ascii?Q?vmD9fqn/wqXGDcIlRIu5jZrbLRtgB8kDwqg6HH4J5b9UuopngJK/vu6cmbvb?= =?us-ascii?Q?/lHATvBn+MpNu9s3UfbRnN9h/6pRVMqnrATUe60lV1PODG0kXITsSC8sSMt3?= =?us-ascii?Q?79ByOue1Txa6A4XuCmniGKPBGWVtZS7udQtFwVIwYSfpr3Zbiiid3eld67iq?= =?us-ascii?Q?X9dwMA3JLDZNyA4sVPoUmTqaLw7mbGw5ypmuLUi/js/gQYy/ljowr1bMUtJS?= =?us-ascii?Q?f5VsSCiZkZkCR66rLXgpIc9ZR7KpA+mGohyESEWzX26oTC3p3WFmZVzuEtUn?= =?us-ascii?Q?aUFRO6QEIKTC8ZI/1nwMP9hEGVLsK+sZAqi4Lj1nhOj20n0qg8YbdbNbwUqb?= =?us-ascii?Q?CK0uJzty/4Ibvkmp8La6PZSbcc5IQ7R5GhM9LXCjsXCpeaL07xaWhgrJ0ZTL?= =?us-ascii?Q?tmMr0disRxTSVDtKo6KFDEjOqQZm7t2Mn+heq4VORSdWc9qcx3D2I4Q2EUX6?= =?us-ascii?Q?BfLW/xrEYoojhJqsfr6Vd3eJ+ARElMjrknmp8qX2m069v24Gr0zA8owPV0HG?= =?us-ascii?Q?Rfru6E7mZUxia13zk8COZHzbmyTfLeld0DsOeNAr+FzZ4vRuX1YR6eo4FVt2?= =?us-ascii?Q?BRWJKark/8Tf1i+Cr8bmnLzqBjI1mFyGiEAAESjhzs0sTZIk5LXV8cxI74DL?= =?us-ascii?Q?TgV94FMb4wE14jzv0IXY36yirhYZhJxVoR4bd8t3UqJJ6G/cDezGR20cDE79?= =?us-ascii?Q?aqMLg7BESSoL9QBHz08LjhStR97TfKNY7e8nwGNOX/LiHk/Is2SX+I128vVc?= =?us-ascii?Q?lX1lx6FqB8rxGGM5OjhV1oaRDwIDnAuHMa7W5Os4f8oL0gcXgWFkP7ZK/IPl?= =?us-ascii?Q?UhrIIVGI8L3yEtV2lvfm/X/Fb0rexXuJMz2Bb/9ErU7HxbP8fnJhkITDKel3?= =?us-ascii?Q?3I4Qru37mih3LcU8avFTVYVH3U7toFEEoPAv1i7NsYGGFDgM0QjDhm0PRr/+?= =?us-ascii?Q?bu3qESSxo4QPHtUKd4QKvtMXjhHKg80vSz5bIp2J7GPa919MjHhOu2bPC3GS?= =?us-ascii?Q?Y2wjzhejPNFU4VDoc8LX/pqp5x8yiyM0a0BRHlQVigsiKRbD0PKVdvn9+Iy1?= =?us-ascii?Q?YuZFINHSuptXxlbhThq7biB+MoZkD+Z//CjeYHgR2U4M85uyrORc6DpLsJ6X?= =?us-ascii?Q?7/A1dcM7uzZ6Pn0J/AqIqdu3AJ1HrrhrRBM9afEjwIbYcyk+V3bkQx5ciNa6?= =?us-ascii?Q?C9PBrbCRVKti8W3vXoR0Gg39gs26Dx3p+U4xCQ0q8jusF29IYYZjhXAJ+Ev0?= =?us-ascii?Q?BblYPJZjyd3SQJ+YxfFnEyeV/WbvSuBmfLqOjzjF?= Content-Type: text/plain; charset="us-ascii" Content-Transfer-Encoding: quoted-printable MIME-Version: 1.0 X-MS-Exchange-CrossTenant-AuthAs: Internal X-MS-Exchange-CrossTenant-AuthSource: DM4PR11MB5994.namprd11.prod.outlook.com X-MS-Exchange-CrossTenant-Network-Message-Id: df99c455-cf9a-49bc-edfd-08db0e2d97da X-MS-Exchange-CrossTenant-originalarrivaltime: 14 Feb 2023 01:48:38.6925 (UTC) X-MS-Exchange-CrossTenant-fromentityheader: Hosted X-MS-Exchange-CrossTenant-id: 46c98d88-e344-4ed4-8496-4ed7712e255d X-MS-Exchange-CrossTenant-mailboxtype: HOSTED X-MS-Exchange-CrossTenant-userprincipalname: 33ELVkTPCPSUBV8z0Ry6clFYlkoUpdTqBHbCOeHlxFQNITmKfRZg7tqgo2gVFgWXiMkGjmTPwN2a0Vw66BkqEw== X-MS-Exchange-Transport-CrossTenantHeadersStamped: IA0PR11MB7695 X-OriginatorOrg: intel.com X-BeenThere: dev@dpdk.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: DPDK patches and discussions List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: dev-bounces@dpdk.org > -----Original Message----- > From: Lu, Wenzhuo > Sent: Wednesday, December 14, 2022 10:06 AM > To: mschmidt ; dev@dpdk.org > Cc: Richardson, Bruce ; Wu, Jingjing > ; Xing, Beilei ; Wang, Haiy= ue > > Subject: RE: [PATCH] net/iavf: fix mbuf VLAN offload flags in the L2TAG2 > path with AVX2 >=20 >=20 >=20 > > -----Original Message----- > > From: Michal Schmidt > > Sent: Thursday, December 8, 2022 8:19 PM > > To: dev@dpdk.org > > Cc: Richardson, Bruce ; Wu, Jingjing > > ; Xing, Beilei ; Wang, > > Haiyue > > Subject: [PATCH] net/iavf: fix mbuf VLAN offload flags in the L2TAG2 > > path with > > AVX2 > > > > It has been observed that mbufs of some received VLAN packets had the > > VLAN tag correctly set in vlan_tci, but ol_flags were missing the > > VLAN-indicating flags. > > > > _mm256_shuffle_epi8 operates as two independent 128-bit operations, > > not as a single 256-bit operation. To have the RTE_MBUF_F_RX_VLAN* > > flags reflected in the resulting vlan_flags for all 8 rx descriptors, > > the input l2tag2_flags_shuf must contain the required pattern in both 1= 28- > bit halves. > > > > Fixes: 3a1aca384d3a ("net/iavf: fix VLAN tag extraction handling") > > > > Signed-off-by: Michal Schmidt > Acked-by: Wenzhuo Lu Applied to dpdk-next-net-intel. Thanks Qi