| /dpdk/drivers/net/bnxt/ |
| H A D | bnxt_rxtx_vec_avx2.c | 168 t1 = _mm256_shuffle_epi8(t1, dsc_shuf_msk); in recv_burst_vec_avx2()
169 rxcmp6_7 = _mm256_blend_epi32(t0, t1, 0x66); in recv_burst_vec_avx2()
173 t1 = _mm256_shuffle_epi8(t1, dsc_shuf_msk); in recv_burst_vec_avx2()
174 rxcmp4_5 = _mm256_blend_epi32(t0, t1, 0x66); in recv_burst_vec_avx2()
178 t1 = _mm256_shuffle_epi8(t1, dsc_shuf_msk); in recv_burst_vec_avx2()
179 rxcmp2_3 = _mm256_blend_epi32(t0, t1, 0x66); in recv_burst_vec_avx2()
183 t1 = _mm256_shuffle_epi8(t1, dsc_shuf_msk); in recv_burst_vec_avx2()
184 rxcmp0_1 = _mm256_blend_epi32(t0, t1, 0x66); in recv_burst_vec_avx2()
189 flags_type = _mm256_unpacklo_epi64(t0, t1); in recv_burst_vec_avx2()
197 flags2 = _mm256_unpackhi_epi64(t0, t1); in recv_burst_vec_avx2()
[all …]
|
| H A D | bnxt_rxtx_vec_neon.c | 83 uint64x2_t t0, t1; in descs_to_mbufs() local
91 t1 = vreinterpretq_u64_u32(vzip1q_u32(mm_rxcmp[2], mm_rxcmp[3])); in descs_to_mbufs()
94 vget_low_u64(t1))); in descs_to_mbufs()
100 t1 = vreinterpretq_u64_u32(vzip1q_u32(mm_rxcmp1[2], mm_rxcmp1[3])); in descs_to_mbufs()
103 vget_low_u64(t1))); in descs_to_mbufs()
124 vget_low_u64(t1))); in descs_to_mbufs()
218 uint64x2_t t0, t1; in recv_burst_vec_neon() local
223 t1 = vld1q_u64((void *)&rxr->rx_buf_ring[mbcons + 2]); in recv_burst_vec_neon()
225 vst1q_u64((void *)&rx_pkts[i + 2], t1); in recv_burst_vec_neon()
252 t1 = vreinterpretq_u64_u32(vzip2q_u32(rxcmp1[2], rxcmp1[3])); in recv_burst_vec_neon()
[all …]
|
| H A D | bnxt_rxtx_vec_sse.c | 74 __m128i t0, t1, flags_type, flags2, index, errors, rss_flags; in descs_to_mbufs() local
83 t1 = _mm_unpacklo_epi32(mm_rxcmp[2], mm_rxcmp[3]); in descs_to_mbufs()
84 flags_type = _mm_unpacklo_epi64(t0, t1); in descs_to_mbufs()
89 t1 = _mm_unpacklo_epi32(mm_rxcmp1[2], mm_rxcmp1[3]); in descs_to_mbufs()
90 flags2 = _mm_unpacklo_epi64(t0, t1); in descs_to_mbufs()
106 t1 = _mm_unpackhi_epi32(mm_rxcmp1[2], mm_rxcmp1[3]); in descs_to_mbufs()
113 errors = _mm_srli_epi32(_mm_unpacklo_epi64(t0, t1), 4); in descs_to_mbufs()
|
| /dpdk/lib/acl/ |
| H A D | acl_run_avx2.h | 94 ymm_t t0, t1; in acl_process_matches_avx2x8() local
123 t1 = _mm256_set_epi64x(tr[7], tr[6], tr[3], tr[2]); in acl_process_matches_avx2x8()
126 ACL_TR_HILO(mm256, __m256, t0, t1, lo, hi); in acl_process_matches_avx2x8()
169 ymm_t t0, t1; in search_avx2x16() local
181 t1 = _mm256_set_epi64x(index_array[7], index_array[6], in search_avx2x16()
184 ACL_TR_HILO(mm256, __m256, t0, t1, tr_lo[0], tr_hi[0]); in search_avx2x16()
188 t1 = _mm256_set_epi64x(index_array[15], index_array[14], in search_avx2x16()
191 ACL_TR_HILO(mm256, __m256, t0, t1, tr_lo[1], tr_hi[1]); in search_avx2x16()
|
| /dpdk/lib/eal/windows/include/ |
| H A D | pthread.h | 51 pthread_equal(pthread_t t1, pthread_t t2) in pthread_equal() argument
53 return t1 == t2; in pthread_equal()
|
| /dpdk/app/test/ |
| H A D | test_acl.c | 678 struct rte_acl_field t1, t2; in convert_rule_3() local
682 t1 = ro->field[RTE_ACL_IPV4VLAN_VLAN1_FIELD]; in convert_rule_3()
690 ro->field[RTE_ACL_IPV4VLAN_SRCP_FIELD] = t1; in convert_rule_3()
844 struct rte_acl_field_def t1, t2; in convert_config_3() local
848 t1 = cfg->defs[RTE_ACL_IPV4VLAN_VLAN1_FIELD]; in convert_config_3()
854 cfg->defs[RTE_ACL_IPV4VLAN_VLAN1_FIELD].field_index = t1.field_index; in convert_config_3()
855 cfg->defs[RTE_ACL_IPV4VLAN_VLAN1_FIELD].input_index = t1.input_index; in convert_config_3()
863 cfg->defs[RTE_ACL_IPV4VLAN_SRCP_FIELD].type = t1.type; in convert_config_3()
864 cfg->defs[RTE_ACL_IPV4VLAN_SRCP_FIELD].size = t1.size; in convert_config_3()
865 cfg->defs[RTE_ACL_IPV4VLAN_SRCP_FIELD].offset = t1.offset; in convert_config_3()
|
| /dpdk/examples/ptpclient/ |
| H A D | ptpclient.c | 333 uint64_t t1 = 0; in delta_eval() local
338 t1 = timespec64_to_ns(&ptp_data->tstamp1); in delta_eval()
343 delta = -((int64_t)((t2 - t1) - (t4 - t3))) / 2; in delta_eval()
|
| /dpdk/doc/guides/sample_app_ug/ |
| H A D | eventdev_pipeline.rst | 39 * ``-t1``: core mask 0x1 for TX
51 -- -r1 -t1 -e4 -w FF00 -s4 -n0 -c32 -W1000 -D
|
| /dpdk/doc/guides/prog_guide/ |
| H A D | env_abstraction_layer.rst | 803 The following is a simple example of cgroup control usage, there are two pthreads(t0 and t1) doing …
816 echo $t1 > /sys/fs/cgroup/cpu/pkt_io/tasks
817 echo $t1 > /sys/fs/cgroup/cpuset/pkt_io/tasks
|
| /dpdk/doc/guides/testpmd_app_ug/ |
| H A D | testpmd_funcs.rst | 5560 clang -O2 -target bpf -c t1.c
5562 Then to load (and JIT compile) t1.o at RX queue 0, port 1:
5566 testpmd> bpf-load rx 1 0 J ./dpdk.org/examples/bpf/t1.o
5568 To load (not JITed) t1.o at TX queue 0, port 0:
5572 testpmd> bpf-load tx 0 0 - ./dpdk.org/examples/bpf/t1.o
|