* |WARNING| pw128643 [PATCH v5 1/3] net/iavf: support Rx timestamp offload on AVX512
[not found] <20230614014948.3495063-2-zhichaox.zeng@intel.com>
@ 2023-06-14 1:43 ` checkpatch
0 siblings, 0 replies; only message in thread
From: checkpatch @ 2023-06-14 1:43 UTC (permalink / raw)
To: test-report; +Cc: Zhichao Zeng
Test-Label: checkpatch
Test-Status: WARNING
http://dpdk.org/patch/128643
_coding style issues_
WARNING:LONG_LINE: line length of 101 exceeds 100 columns
#159: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:636:
+ hw_low_last = _mm256_set_epi32(0, 0, 0, 0, 0, 0, 0, (uint32_t)rxq->phc_time);
WARNING:LONG_LINE: line length of 110 exceeds 100 columns
#209: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1317:
+ __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
#211: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1319:
+ __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
#214: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1322:
+ ts_low = _mm256_or_si256(ts_low, _mm256_srli_si256(ts, 3 * 4));
WARNING:LONG_LINE: line length of 103 exceeds 100 columns
#216: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1324:
+ ts_low = _mm256_or_si256(ts_low, _mm256_srli_si256(ts, 2 * 4));
WARNING:LONG_LINE: line length of 103 exceeds 100 columns
#222: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1330:
+ ts_low1 = _mm256_permutevar8x32_epi32(ts_low, ts_permute_mask);
WARNING:LONG_LINE: line length of 106 exceeds 100 columns
#224: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1332:
+ _mm256_set_epi32(6, 5, 4, 3, 2, 1, 0, 7));
WARNING:LONG_LINE: line length of 127 exceeds 100 columns
#226: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1334:
+ _mm256_set_epi32(mask, mask, mask, mask, mask, mask, mask, 0));
WARNING:LONG_LINE: line length of 109 exceeds 100 columns
#229: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1337:
+ _mm256_set_epi32(0, 0, 0, 0, 0, 0, 0, mask));
WARNING:LONG_LINE: line length of 127 exceeds 100 columns
#232: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1340:
+ iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 0);
WARNING:LONG_LINE: line length of 127 exceeds 100 columns
#234: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1342:
+ iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 1);
WARNING:LONG_LINE: line length of 127 exceeds 100 columns
#236: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1344:
+ iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 2);
WARNING:LONG_LINE: line length of 127 exceeds 100 columns
#238: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1346:
+ iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 3);
WARNING:LONG_LINE: line length of 127 exceeds 100 columns
#240: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1348:
+ iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 4);
WARNING:LONG_LINE: line length of 127 exceeds 100 columns
#242: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1350:
+ iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 5);
WARNING:LONG_LINE: line length of 127 exceeds 100 columns
#244: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1352:
+ iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 6);
WARNING:LONG_LINE: line length of 127 exceeds 100 columns
#246: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1354:
+ iavf_timestamp_dynfield_offset, uint32_t *) = _mm256_extract_epi32(ts_low1, 7);
WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring
#251: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1359:
+ if (iavf_get_phc_time(rxq))
WARNING:LONG_LINE: line length of 124 exceeds 100 columns
#254: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1362:
+ iavf_timestamp_dynfield_offset, uint32_t *);
WARNING:LONG_LINE: line length of 121 exceeds 100 columns
#255: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1363:
+ rxq->phc_time = iavf_tstamp_convert_32b_64b(rxq->phc_time, in_timestamp);
WARNING:LONG_LINE: line length of 130 exceeds 100 columns
#259: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1367:
+ iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32);
WARNING:LONG_LINE: line length of 130 exceeds 100 columns
#261: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1369:
+ iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32);
WARNING:LONG_LINE: line length of 130 exceeds 100 columns
#263: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1371:
+ iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32);
WARNING:LONG_LINE: line length of 130 exceeds 100 columns
#265: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1373:
+ iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32);
WARNING:LONG_LINE: line length of 130 exceeds 100 columns
#267: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1375:
+ iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32);
WARNING:LONG_LINE: line length of 130 exceeds 100 columns
#269: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1377:
+ iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32);
WARNING:LONG_LINE: line length of 130 exceeds 100 columns
#271: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1379:
+ iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32);
WARNING:LONG_LINE: line length of 130 exceeds 100 columns
#273: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1381:
+ iavf_timestamp_dynfield_offset + 4, uint32_t *) = (uint32_t)(rxq->phc_time >> 32);
WARNING:LONG_LINE: line length of 118 exceeds 100 columns
#276: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1384:
+ cmp_ret = _mm256_andnot_si256(_mm256_cmpeq_epi32(max_ret, ts_low1), cmp_mask);
WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring
#282: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1390:
+ while (shift > 1) {
WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring
#286: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1394:
+ switch (shift) {
WARNING:LONG_LINE: line length of 128 exceeds 100 columns
#288: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1396:
+ mask_low = _mm256_set_epi32(0, 0, 0, 0, mask, mask, mask, mask);
WARNING:LONG_LINE: line length of 129 exceeds 100 columns
#289: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1397:
+ mask_high = _mm256_set_epi32(mask, mask, mask, mask, 0, 0, 0, 0);
WARNING:LONG_LINE: line length of 110 exceeds 100 columns
#292: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1400:
+ mask_low = _mm256_srli_si256(cmp_mask, 2 * 4);
WARNING:LONG_LINE: line length of 111 exceeds 100 columns
#293: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1401:
+ mask_high = _mm256_slli_si256(cmp_mask, 2 * 4);
WARNING:LONG_LINE: line length of 110 exceeds 100 columns
#296: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1404:
+ mask_low = _mm256_srli_si256(cmp_mask, 1 * 4);
WARNING:LONG_LINE: line length of 111 exceeds 100 columns
#297: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1405:
+ mask_high = _mm256_slli_si256(cmp_mask, 1 * 4);
WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring
#301: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1409:
+ if (ret) {
WARNING:LONG_LINE: line length of 109 exceeds 100 columns
#302: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1410:
+ ret = _mm256_testz_si256(cmp_ret, mask_high);
WARNING:DEEP_INDENTATION: Too many leading tabs - consider code refactoring
#305: FILE: drivers/net/iavf/iavf_rxtx_vec_avx512.c:1413:
+ } else {
total: 0 errors, 40 warnings, 0 checks, 289 lines checked
^ permalink raw reply [flat|nested] only message in thread