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 30B82A0548; Thu, 2 Jun 2022 20:42:04 +0200 (CEST) Received: from [217.70.189.124] (localhost [127.0.0.1]) by mails.dpdk.org (Postfix) with ESMTP id A8A3740691; Thu, 2 Jun 2022 20:42:04 +0200 (CEST) Received: from mga01.intel.com (mga01.intel.com [192.55.52.88]) by mails.dpdk.org (Postfix) with ESMTP id DB65E4021E; Thu, 2 Jun 2022 20:42:02 +0200 (CEST) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=intel.com; i=@intel.com; q=dns/txt; s=Intel; t=1654195323; x=1685731323; h=message-id:date:subject:to:cc:references:from: in-reply-to:content-transfer-encoding:mime-version; bh=RCXFT3aDQVefm/HTTvp4vgNpnM7faWc9WYY6w5c/E3Q=; b=Imh5fg5DjZSzQ5R01M82kOY/00PBLWxQ3Jae68KwTY9m7N7oSWx8I7wI 5j0l9kNWtdELXTZif70UD5Q5/0LyYhp4UlqkjVH6+6QqWsgNp4auDMze6 Zf5iJcScneTbDlrBwPgPY/TJMG7oQ0m12P3S4kVSRwoB5D3Sfcr/EsXid URg0+X2F7/b2mkTE007jx6PVGGxMxJ98E9Rjvum+2144Q7qnE2oI3wY5L D9CFEi7RngV62ljQk/Gq5Y9zlvmLzYthGOsF7/SnXtoGi4WLgpA55f8/j r9zsNcDyCiBqHmkc7fmd5w5ZHrrgXxb0H0odRK5dlbNW9GHy1zX8GaHs+ Q==; X-IronPort-AV: E=McAfee;i="6400,9594,10366"; a="301410639" X-IronPort-AV: E=Sophos;i="5.91,272,1647327600"; d="scan'208";a="301410639" Received: from fmsmga003.fm.intel.com ([10.253.24.29]) by fmsmga101.fm.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 02 Jun 2022 11:42:01 -0700 X-ExtLoop1: 1 X-IronPort-AV: E=Sophos;i="5.91,272,1647327600"; d="scan'208";a="668114537" Received: from orsmsx601.amr.corp.intel.com ([10.22.229.14]) by FMSMGA003.fm.intel.com with ESMTP; 02 Jun 2022 11:42:01 -0700 Received: from orsmsx602.amr.corp.intel.com (10.22.229.15) 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.2308.27; Thu, 2 Jun 2022 11:42:01 -0700 Received: from orsedg603.ED.cps.intel.com (10.7.248.4) by orsmsx602.amr.corp.intel.com (10.22.229.15) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_128_GCM_SHA256) id 15.1.2308.27 via Frontend Transport; Thu, 2 Jun 2022 11:42:01 -0700 Received: from NAM10-DM6-obe.outbound.protection.outlook.com (104.47.58.100) by edgegateway.intel.com (134.134.137.100) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.1.2308.27; Thu, 2 Jun 2022 11:42:00 -0700 ARC-Seal: i=1; a=rsa-sha256; s=arcselector9901; d=microsoft.com; cv=none; b=NrHrSM6UdLX1k2GfQKuri5mhjCI0Q/b9k0STUQcYFAJWWVm20QQTKL1orG8JQ2MOuBpbEDCoEQsqgU9C71PUXAbbVBcsAdzABclPl8iSi5NPuJr6cAxr+D6HPsrNpgt/1DkuQSl54b2lw8TDuu5AKXjb8qhAsBg7181ZNsHk6HS+t9ADCqs3zmAmN/gbUvvhAV7IHzgJ8aL2Kt/GiUSYtwp0c0PqQNuAhvNEaYwu45zE+4Yu/ozvcf7UDWmbKBu4E3COTT3mfAP1haDktOSY2v1mMTONsKHIBC3BJ2nK43lukJArTSfc+Ios6JVcHfN+Q0qzVz08F31eau5CAIx6DA== 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=3W0+aJ9KRZaQHhIpJUdXUaT20bNlW1pC3gR/8D0bBok=; b=kuCR85zQ5uBLmjBDDbl3Yri7CE1EzWb7fJ3RtfgBsjwL7Yk4owheCWlv0i0H5NN7KI/wkDtTew8ZP77wW/CoJmyHucQ3zA3+7xy7EptwZD+pigIJtU8h9mpteFcgubkkRTsIrAo+z78Wr1S43gLnjgDWcmxV0sINor0vBt+6yl66rMCyxwD3w55jHnAaGm8pMlH5wzrVGwqZTfpwdl5N3Md6oRKljx7B68GCoA0mgvqJKPo9jU9I/s14RuH9WGEgDiYhmimAPsdNT95+2Fj3ihuv3XSfufnZKfE6HVxOL60NMKEvG66V1fwpzu7hTR7LHgCYfGB7PdiW5rm5VEu1Kw== 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 Authentication-Results: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=intel.com; Received: from SJ0PR11MB5772.namprd11.prod.outlook.com (2603:10b6:a03:422::8) by SA2PR11MB4827.namprd11.prod.outlook.com (2603:10b6:806:11f::19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.5314.13; Thu, 2 Jun 2022 18:41:54 +0000 Received: from SJ0PR11MB5772.namprd11.prod.outlook.com ([fe80::64ab:a179:cce5:11d0]) by SJ0PR11MB5772.namprd11.prod.outlook.com ([fe80::64ab:a179:cce5:11d0%7]) with mapi id 15.20.5314.013; Thu, 2 Jun 2022 18:41:54 +0000 Message-ID: Date: Thu, 2 Jun 2022 19:41:48 +0100 User-Agent: Mozilla/5.0 (Windows NT 10.0; Win64; x64; rv:91.0) Gecko/20100101 Firefox/91.0 Thunderbird/91.9.1 Subject: Re: [PATCH 12/12] test/ipsec: fix build with GCC 12 Content-Language: en-US To: David Marchand , CC: , , , Konstantin Ananyev , Bernard Iremonger References: <20220518101657.1230416-1-david.marchand@redhat.com> <20220518101657.1230416-13-david.marchand@redhat.com> From: "Medvedkin, Vladimir" In-Reply-To: <20220518101657.1230416-13-david.marchand@redhat.com> Content-Type: text/plain; charset="UTF-8"; format=flowed Content-Transfer-Encoding: 8bit X-ClientProxiedBy: DB6P191CA0008.EURP191.PROD.OUTLOOK.COM (2603:10a6:6:28::18) To SJ0PR11MB5772.namprd11.prod.outlook.com (2603:10b6:a03:422::8) MIME-Version: 1.0 X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id: 4516d096-4908-490a-7d2d-08da44c79075 X-MS-TrafficTypeDiagnostic: SA2PR11MB4827:EE_ X-Microsoft-Antispam-PRVS: X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam: BCL:0; X-Microsoft-Antispam-Message-Info: ka7t/2t1KXe9gAFcx7YTCRcePD7bLFB/SfuU5OO9veDkYKENBJMajDy8din3SqQAQuHmNJBePV7O7Qqx8sO+lmJYn9cxERkntl+ojKe1nijm+uV3lfmvxAD9PIYu+EbO5or1c4KzJ8dhZSf5bQSM+sND74oqY/wjw3A/cp4JcYhm3hKj8Fm3k8IN7daHROUbPwL7kpG4RTAzUVzI8EPcQEbGOlBquDoYZk+rDUpwEsW7z+n8qpp27EFu3zxCCpgv4Hn2H1x4bbO8swNr1OWsD95kFnDW8zhr2fLZ8wNVQWasYSwbNGTxueinvfuOMQ6nuAHHD/6af5zCBlAZZQF3JNr0hFsH+MYlMOe7tsqL0dYAAUKCazZW/FpJybbGaF7+FQmDGhAibRvF1rZhtBn7r/1wWqRV8xu62hqQ35l+rynm7xGTqgZAE6o2ZyjbabwQUnAwgnv8jt41XJAqRpGq8eapawZeImkghGFlL0w23rc6BeXQc1B4vdTOsjeRfc9HnkzcfzAup/v7W3nuCIW0MOad0qKfFBBZBBZvmf+SzUeyUA0L7Pl8E/5V5Qb7PFRr0iIjn+D4ZcSxi8+t1MV7MHbL8XK1N1w+1Ms483iRK1roHC1ZbmBmFP/rp8vGMqiNE0N6VaYWUtIcEaL+WHS0LWESA1/RTLWUXsgd8S7UO4aDOSTZzMGR9RmzFj1h+Y1erZZlwJpkePLKpksdzWgY30pTq7X1byNtbWotUSm17kE= X-Forefront-Antispam-Report: CIP:255.255.255.255; CTRY:; LANG:en; SCL:1; SRV:; IPV:NLI; SFV:NSPM; H:SJ0PR11MB5772.namprd11.prod.outlook.com; PTR:; CAT:NONE; SFS:(13230001)(366004)(66946007)(2616005)(316002)(26005)(54906003)(36756003)(38100700002)(66556008)(508600001)(5660300002)(31686004)(8936002)(2906002)(6666004)(4326008)(8676002)(82960400001)(6486002)(66476007)(6512007)(86362001)(107886003)(83380400001)(186003)(31696002)(53546011)(6506007)(43740500002)(45980500001); DIR:OUT; SFP:1102; X-MS-Exchange-AntiSpam-MessageData-ChunkCount: 1 X-MS-Exchange-AntiSpam-MessageData-0: =?utf-8?B?aDY5c3R4RzMzY25wZm90QzJBSHNBUFBwMEVIcU9KSjQ5VkZCckp2dkp4Mzll?= =?utf-8?B?Y0Frdko1N0s2TTlYSEZHM0xaMUlMYXVQeEp0ZS9sM1dnWkVGUzlkaEZBSVE2?= =?utf-8?B?N1BFV1R6L2xOYzE1S2tZVXJkTmZrUXN2M2xJenlFREZNZmlrWDBTcS8yYnNY?= =?utf-8?B?bU5FWXcyYnk3WFBKaExvVG5GdzEyeWdHbTRvLzhXZFB5RE4zblVibkhGWno5?= =?utf-8?B?UzNuMWlVSmFCcEhwRXQ2bURvWTlvRTNoUVhoOXJRQU1ZSjdzVTZsdHZQc0c5?= =?utf-8?B?NFJBLzdVN3YvdTZneFhUa0VMNWltRjJKaU9kdHpoZnZmUmpJZ1hONXhaZWJr?= =?utf-8?B?aXdSbGZIamk1LytUN21SRlk0SzFiU01RSGpUNnNiMHNYWWkwOFRLRlJueURn?= =?utf-8?B?Mm0ySFRaRUtsWTg3SmFUd2o4NmNNZ3h4RWgrTk4zT3IxNnk2Qmh3ejJwcWpt?= =?utf-8?B?SnY4SER5Z2plZGlRbXVmOWoxMTE2UW5ndnRBZm1qR3B6M3NMdzVPSWIrZzBS?= =?utf-8?B?eXBTd2luZDV2UlVFVmcrOVhWUS9qaWIrYUlWU09iVHpkd2l3bDBMZU1qTGJm?= =?utf-8?B?UnhyQ0hsNUZ5RElvVWZ2OW80ditaaGdjYzRDNHNycWR3RGlRaEJ3SHlmOXFX?= =?utf-8?B?SFphUUQrWHZJN1NXSFZmY0NFc3loVDJIQnJwYmQzTm14TG1ySmNKNFo5TTRy?= =?utf-8?B?RFhMNlUzWGNCYkx2c2lheWZYbW9wMTQwdVV4dEdsZDhYckphYi9iMURDbmY1?= =?utf-8?B?TGpKMy9mdDJpZjVKd3ZhK1hjamh6dVI0elU2amxyQnNsOXhwMFJDb0w5ODdQ?= =?utf-8?B?MlhveUlCQmZjc1EzTnpkY3NSbjUyT1pMaUoyUnMxQm1yVHBESHpkYythRTVV?= =?utf-8?B?KzhVS2UxMnU2aVVBcEhNbFJxaUg3Nkg5dHpGeVdoczZvMGJyU25LaWZJQkk5?= =?utf-8?B?WlVFT2EwNTZxUU4rZHdoeGRIQ3RvTWRHU1d4NFJFQ1NYQnBlZ0p6MVZDaThN?= =?utf-8?B?QzhiOXBRb01PS08rS3NQUmV4RE81ZkJjeGJJV0xuNE1mKzRPdkprNGpOZlEy?= =?utf-8?B?Q250RmxZS0ZUeU1aOGNkY2I1NDdWOVFrTlRyOG9JS2IrNXh1WEtBaXo5NFcx?= =?utf-8?B?eUwySkpScFluRXI5emxPcUFEeVYrZ1VpVnQvTjdFeUd6dHA2amppQWk3M3M4?= =?utf-8?B?eStHODFwYWFvM3ZEVkZXWHRjMUpqZm9OYlFwa0R5Y1BxOWgrbWxKSktDd2E5?= =?utf-8?B?ZjRtQUVRcjc1Ykx3Wjd4dVpadGVBMDFIM1NRVEdrS3M0dXhpTkNFSzBTY0JY?= =?utf-8?B?dVJmeVNoaWxmQ2o0blJHOGdrMWlmVklCbzNIdDRreHc4bG9CUWthTEl6ZE5F?= =?utf-8?B?OHd5Z0dhcEhCS0pEb3N4Rm5KcDJLZGVRLzFZVDE4aXNNeEZBRy9mb1pJT0tU?= =?utf-8?B?YTlabDF2Lzl0bTBqb1JwcmVOd1ZNekpudHBzdU96dUZwK3I1VkJ3Nzhnd0da?= =?utf-8?B?ek02bXFuV2hiU3JLd09TVVRCTy9CWU85UWFFYnlLSVRjRHRzS3daVTNheXZU?= =?utf-8?B?QnovdkRncWpTUm4yU213K25WVE0zK1hoT3RpdnBOTVE5SkRpakQ1MGNhMlBn?= =?utf-8?B?ZmFySUwza2FDODhGSnR3czVHN2FKMmErb1ZxUVJDOHZ5MzZPbHFQdlJOOFVU?= =?utf-8?B?VVVuZkdRa0ZyRDNDajFFTWpnNE01ZzlmWHVYcGljajNvL2UvQ1RYaW52MUcx?= =?utf-8?B?eU40SERmZGhPR2Vrdm4za3FhUlBGd1FScFFJVUpDTmowUWFNSmo4cXdnYXJz?= =?utf-8?B?ajVBTnBPRTZGMjVkY2lwWUk1WmY1Y0E3amhyeFpmdE1XNkxJUDNpYlhaano0?= =?utf-8?B?VFVNU2UwSmRtQ0NsOXVyaTZQTGV3RUoyV0VUamlTV3VieEd0WmdSdUFHYjlO?= =?utf-8?B?V1kxRXhxcEFiY0R5R2k3RWo3VGRiZHlOZk5QUHp4Z0F2RTVIdGpnQTFzMXVF?= =?utf-8?B?czRhNlJzZnlEdGw0TTIxbzhzYnFtSi9SR1FYWVR3aWQ3U1NEelhaU2Y3ZDJv?= =?utf-8?B?K2RFU244RnRXak5pQXNUVzYwc1NoNUlXNWVKYWFneElVaHY2Q2Z4OW44a1Rt?= =?utf-8?B?dVl5ZngwQWVkUW50M21qK0JOQnRrUW9KYlhrWHlOSENkS3hrMW5ESng3R1Qx?= =?utf-8?B?MjNaN01zR2w1andvNkUrRUlWSE5vYjQ0YXFTcGFEK014YzdYRmJ4UU5TcVhy?= =?utf-8?B?SDN6ZmtzVitLL2tpOGZKWkIxS1NLelhtOVQzck5RbDRzN2JYd2QvTnV5MzVG?= =?utf-8?B?Y2xNaFdlT3JteWl6WDdubUx1UkdyZmhuakx3VVM0eVVJOSt5S2FIdnphY1Jy?= =?utf-8?Q?RGpqDpRKGUfLMq6A=3D?= X-MS-Exchange-CrossTenant-Network-Message-Id: 4516d096-4908-490a-7d2d-08da44c79075 X-MS-Exchange-CrossTenant-AuthSource: SJ0PR11MB5772.namprd11.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Internal X-MS-Exchange-CrossTenant-OriginalArrivalTime: 02 Jun 2022 18:41:54.3363 (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: 8SoxqBbHyJlflDsLTMXkGWFjzOfgPVqYz35kiRu5NEvXD6MAebahKE8kwQWCZEaIc1GBsxx3QkczID1/mbjHzB5dgtmUKkJThGeqH4jWSdY= X-MS-Exchange-Transport-CrossTenantHeadersStamped: SA2PR11MB4827 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 Hi David, On 18/05/2022 11:16, David Marchand wrote: > GCC 12 raises the following warning: > > In function ‘_mm256_loadu_si256’, > inlined from ‘rte_mov32’ at > ../lib/eal/x86/include/rte_memcpy.h:319:9, > inlined from ‘rte_mov128’ at > ../lib/eal/x86/include/rte_memcpy.h:344:2, > inlined from ‘rte_memcpy_generic’ at > ../lib/eal/x86/include/rte_memcpy.h:438:4, > inlined from ‘rte_memcpy’ at > ../lib/eal/x86/include/rte_memcpy.h:882:10, > inlined from ‘setup_test_string.constprop’ at > ../app/test/test_ipsec.c:572:4: > /usr/lib/gcc/x86_64-redhat-linux/12/include/avxintrin.h:929:10: error: > array subscript ‘__m256i_u[3]’ is partly outside array bounds of > ‘const char[108]’ [-Werror=array-bounds] > 929 | return *__P; > | ^~~~ > ../app/test/test_ipsec.c: In function ‘setup_test_string.constprop’: > ../app/test/test_ipsec.c:539:12: note: at offset 96 into object > ‘null_plain_data’ of size 108 > 539 | const char null_plain_data[] = > | ^~~~~~~~~~~~~~~ > > Split copy request into copies of string lengths and remove unused > blocksize. > > Cc: stable@dpdk.org > > Signed-off-by: David Marchand > --- > app/test/test_ipsec.c | 48 ++++++++++++++++++++++++++----------------- > 1 file changed, 29 insertions(+), 19 deletions(-) > > diff --git a/app/test/test_ipsec.c b/app/test/test_ipsec.c > index 8da025bf66..d7455fd021 100644 > --- a/app/test/test_ipsec.c > +++ b/app/test/test_ipsec.c > @@ -554,24 +554,28 @@ struct rte_ipv4_hdr ipv4_outer = { > }; > > static struct rte_mbuf * > -setup_test_string(struct rte_mempool *mpool, > - const char *string, size_t len, uint8_t blocksize) > +setup_test_string(struct rte_mempool *mpool, const char *string, > + size_t string_len, size_t len) > { > struct rte_mbuf *m = rte_pktmbuf_alloc(mpool); > - size_t t_len = len - (blocksize ? (len % blocksize) : 0); > > if (m) { > memset(m->buf_addr, 0, m->buf_len); > - char *dst = rte_pktmbuf_append(m, t_len); > + char *dst = rte_pktmbuf_append(m, len); > > if (!dst) { > rte_pktmbuf_free(m); > return NULL; > } > - if (string != NULL) > - rte_memcpy(dst, string, t_len); > - else > - memset(dst, 0, t_len); > + if (string != NULL) { > + size_t off; > + > + for (off = 0; off + string_len < len; off += string_len) I think it should be off + string_len <= len here, because otherwise, if len is a multiple of string_len, the last ret_memcpy (after this loop) will copy 0 bytes. > + rte_memcpy(&dst[off], string, string_len); > + rte_memcpy(&dst[off], string, len % string_len); > + } else { > + memset(dst, 0, len); > + } > } > > return m; > @@ -1365,7 +1369,8 @@ test_ipsec_crypto_outb_burst_null_null(int i) > /* Generate input mbuf data */ > for (j = 0; j < num_pkts && rc == 0; j++) { > ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool, > - null_plain_data, test_cfg[i].pkt_sz, 0); > + null_plain_data, sizeof(null_plain_data), > + test_cfg[i].pkt_sz); > if (ut_params->ibuf[j] == NULL) > rc = TEST_FAILED; > else { > @@ -1483,7 +1488,8 @@ test_ipsec_inline_crypto_inb_burst_null_null(int i) > /* Generate test mbuf data */ > ut_params->obuf[j] = setup_test_string( > ts_params->mbuf_pool, > - null_plain_data, test_cfg[i].pkt_sz, 0); > + null_plain_data, sizeof(null_plain_data), > + test_cfg[i].pkt_sz); > if (ut_params->obuf[j] == NULL) > rc = TEST_FAILED; > } > @@ -1551,16 +1557,17 @@ test_ipsec_inline_proto_inb_burst_null_null(int i) > > /* Generate inbound mbuf data */ > for (j = 0; j < num_pkts && rc == 0; j++) { > - ut_params->ibuf[j] = setup_test_string( > - ts_params->mbuf_pool, > - null_plain_data, test_cfg[i].pkt_sz, 0); > + ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool, > + null_plain_data, sizeof(null_plain_data), > + test_cfg[i].pkt_sz); > if (ut_params->ibuf[j] == NULL) > rc = TEST_FAILED; > else { > /* Generate test mbuf data */ > ut_params->obuf[j] = setup_test_string( > ts_params->mbuf_pool, > - null_plain_data, test_cfg[i].pkt_sz, 0); > + null_plain_data, sizeof(null_plain_data), > + test_cfg[i].pkt_sz); > if (ut_params->obuf[j] == NULL) > rc = TEST_FAILED; > } > @@ -1660,7 +1667,8 @@ test_ipsec_inline_crypto_outb_burst_null_null(int i) > /* Generate test mbuf data */ > for (j = 0; j < num_pkts && rc == 0; j++) { > ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool, > - null_plain_data, test_cfg[i].pkt_sz, 0); > + null_plain_data, sizeof(null_plain_data), > + test_cfg[i].pkt_sz); > if (ut_params->ibuf[0] == NULL) > rc = TEST_FAILED; > > @@ -1738,15 +1746,16 @@ test_ipsec_inline_proto_outb_burst_null_null(int i) > /* Generate test mbuf data */ > for (j = 0; j < num_pkts && rc == 0; j++) { > ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool, > - null_plain_data, test_cfg[i].pkt_sz, 0); > + null_plain_data, sizeof(null_plain_data), > + test_cfg[i].pkt_sz); > if (ut_params->ibuf[0] == NULL) > rc = TEST_FAILED; > > if (rc == 0) { > /* Generate test tunneled mbuf data for comparison */ > ut_params->obuf[j] = setup_test_string( > - ts_params->mbuf_pool, > - null_plain_data, test_cfg[i].pkt_sz, 0); > + ts_params->mbuf_pool, null_plain_data, > + sizeof(null_plain_data), test_cfg[i].pkt_sz); > if (ut_params->obuf[j] == NULL) > rc = TEST_FAILED; > } > @@ -1815,7 +1824,8 @@ test_ipsec_lksd_proto_inb_burst_null_null(int i) > for (j = 0; j < num_pkts && rc == 0; j++) { > /* packet with sequence number 0 is invalid */ > ut_params->ibuf[j] = setup_test_string(ts_params->mbuf_pool, > - null_encrypted_data, test_cfg[i].pkt_sz, 0); > + null_encrypted_data, sizeof(null_encrypted_data), > + test_cfg[i].pkt_sz); > if (ut_params->ibuf[j] == NULL) > rc = TEST_FAILED; > } -- Regards, Vladimir