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 3AA8142BA9 for ; Fri, 26 May 2023 11:47:37 +0200 (CEST) Received: from mails.dpdk.org (localhost [127.0.0.1]) by mails.dpdk.org (Postfix) with ESMTP id 3717540A89; Fri, 26 May 2023 11:47:37 +0200 (CEST) Received: from dpdk.org (dpdk.org [92.243.24.197]) by mails.dpdk.org (Postfix) with ESMTP id 75D8340A89 for ; Fri, 26 May 2023 11:47:35 +0200 (CEST) Received: by dpdk.org (Postfix, from userid 65534) id 6D285120927; Fri, 26 May 2023 11:47:35 +0200 (CEST) Subject: |WARNING| pw127559 [PATCH v4 2/3] net/iavf: support Rx timestamp offload on AVX2 In-Reply-To: <20230526095055.2855121-3-zhichaox.zeng@intel.com> References: <20230526095055.2855121-3-zhichaox.zeng@intel.com> To: test-report@dpdk.org From: checkpatch@dpdk.org Cc: Zhichao Zeng Message-Id: <20230526094735.6D285120927@dpdk.org> Date: Fri, 26 May 2023 11:47:35 +0200 (CEST) X-BeenThere: test-report@dpdk.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: automatic DPDK test reports List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: test-report-bounces@dpdk.org Test-Label: checkpatch Test-Status: WARNING http://dpdk.org/patch/127559 _coding style issues_ WARNING:LONG_LINE: line length of 110 exceeds 100 columns #163: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1165: + __m256i ts_desp_mask = _mm256_set_epi32(mask, 0, 0, 0, mask, 0, 0, 0); WARNING:LONG_LINE: line length of 107 exceeds 100 columns #165: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1167: + __m256i ts_permute_mask = _mm256_set_epi32(7, 3, 6, 2, 5, 1, 4, 0); WARNING:LONG_LINE: line length of 103 exceeds 100 columns #168: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1170: + ts_low = _mm256_or_si256(ts_low, _mm256_srli_si256(ts, 3 * 4)); WARNING:LONG_LINE: line length of 103 exceeds 100 columns #170: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1172: + ts_low = _mm256_or_si256(ts_low, _mm256_srli_si256(ts, 2 * 4)); WARNING:LONG_LINE: line length of 103 exceeds 100 columns #176: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1178: + ts_low1 = _mm256_permutevar8x32_epi32(ts_low, ts_permute_mask); WARNING:LONG_LINE: line length of 106 exceeds 100 columns #178: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1180: + _mm256_set_epi32(6, 5, 4, 3, 2, 1, 0, 7)); WARNING:LONG_LINE: line length of 127 exceeds 100 columns #180: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1182: + _mm256_set_epi32(mask, mask, mask, mask, mask, mask, mask, 0)); WARNING:LONG_LINE: line length of 109 exceeds 100 columns #183: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1185: + _mm256_set_epi32(0, 0, 0, 0, 0, 0, 0, mask)); WARNING:LONG_LINE: line length of 127 exceeds 100 columns #186: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1188: + iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 0); WARNING:LONG_LINE: line length of 127 exceeds 100 columns #188: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1190: + iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 1); WARNING:LONG_LINE: line length of 127 exceeds 100 columns #190: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1192: + iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 2); WARNING:LONG_LINE: line length of 127 exceeds 100 columns #192: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1194: + iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 3); WARNING:LONG_LINE: line length of 127 exceeds 100 columns #194: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1196: + iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 4); WARNING:LONG_LINE: line length of 127 exceeds 100 columns #196: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1198: + iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 5); WARNING:LONG_LINE: line length of 127 exceeds 100 columns #198: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1200: + iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 6); WARNING:LONG_LINE: line length of 127 exceeds 100 columns #200: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1202: + iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 7); WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring #204: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1206: + if (iavf_get_phc_time(rxq)) WARNING:LONG_LINE: line length of 108 exceeds 100 columns #207: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1209: + iavf_timestamp_dynfield_offset, uint32_t *); WARNING:LONG_LINE: line length of 121 exceeds 100 columns #208: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1210: + rxq->phc_time = iavf_tstamp_convert_32b_64b(rxq->phc_time, in_timestamp); WARNING:LONG_LINE: line length of 130 exceeds 100 columns #212: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1214: + iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32); WARNING:LONG_LINE: line length of 130 exceeds 100 columns #214: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1216: + iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32); WARNING:LONG_LINE: line length of 130 exceeds 100 columns #216: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1218: + iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32); WARNING:LONG_LINE: line length of 130 exceeds 100 columns #218: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1220: + iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32); WARNING:LONG_LINE: line length of 130 exceeds 100 columns #220: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1222: + iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32); WARNING:LONG_LINE: line length of 130 exceeds 100 columns #222: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1224: + iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32); WARNING:LONG_LINE: line length of 130 exceeds 100 columns #224: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1226: + iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32); WARNING:LONG_LINE: line length of 130 exceeds 100 columns #226: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1228: + iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32); WARNING:LONG_LINE: line length of 118 exceeds 100 columns #229: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1231: + cmp_ret = _mm256_andnot_si256(_mm256_cmpeq_epi32(max_ret, ts_low1), cmp_mask); WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring #235: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1237: + while (shift > 1) { WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring #239: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1241: + switch (shift) { WARNING:LONG_LINE: line length of 128 exceeds 100 columns #241: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1243: + mask_low = _mm256_set_epi32(0, 0, 0, 0, mask, mask, mask, mask); WARNING:LONG_LINE: line length of 129 exceeds 100 columns #242: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1244: + mask_high = _mm256_set_epi32(mask, mask, mask, mask, 0, 0, 0, 0); WARNING:LONG_LINE: line length of 110 exceeds 100 columns #245: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1247: + mask_low = _mm256_srli_si256(cmp_mask, 2 * 4); WARNING:LONG_LINE: line length of 111 exceeds 100 columns #246: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1248: + mask_high = _mm256_slli_si256(cmp_mask, 2 * 4); WARNING:LONG_LINE: line length of 110 exceeds 100 columns #249: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1251: + mask_low = _mm256_srli_si256(cmp_mask, 1 * 4); WARNING:LONG_LINE: line length of 111 exceeds 100 columns #250: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1252: + mask_high = _mm256_slli_si256(cmp_mask, 1 * 4); WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring #254: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1256: + if (ret) { WARNING:LONG_LINE: line length of 109 exceeds 100 columns #255: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1257: + ret = _mm256_testz_si256(cmp_ret, mask_high); WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring #258: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1260: + } else { WARNING:LONG_LINE: line length of 124 exceeds 100 columns #263: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1265: + mbuf_flags = _mm256_or_si256(mbuf_flags, _mm256_set1_epi32(iavf_timestamp_dynflag)); WARNING:LONG_LINE: line length of 130 exceeds 100 columns #321: FILE: drivers/net/iavf/iavf_rxtx_vec_avx2.c:1447: + rxq->phc_time = *RTE_MBUF_DYNFIELD(rx_pkts[received - 1], iavf_timestamp_dynfield_offset, rte_mbuf_timestamp_t *); total: 0 errors, 41 warnings, 0 checks, 230 lines checked