Home
last modified time | relevance | path

Searched refs:vecs (Results 1 – 14 of 14) sorted by relevance

/freebsd/contrib/llvm-project/llvm/lib/Support/BLAKE3/
H A Dblake3_avx512.c431 INLINE void transpose_vecs_128(__m128i vecs[4]) { in transpose_vecs_128()
435 __m128i ab_01 = _mm_unpacklo_epi32(vecs[0], vecs[1]); in transpose_vecs_128()
436 __m128i ab_23 = _mm_unpackhi_epi32(vecs[0], vecs[1]); in transpose_vecs_128()
437 __m128i cd_01 = _mm_unpacklo_epi32(vecs[2], vecs[3]); in transpose_vecs_128()
438 __m128i cd_23 = _mm_unpackhi_epi32(vecs[2], vecs[3]); in transpose_vecs_128()
446 vecs[0] = abcd_0; in transpose_vecs_128()
447 vecs[1] = abcd_1; in transpose_vecs_128()
448 vecs[2] = abcd_2; in transpose_vecs_128()
449 vecs[3] = abcd_3; in transpose_vecs_128()
675 INLINE void transpose_vecs_256(__m256i vecs[8]) { in transpose_vecs_256()
[all …]
H A Dblake3_avx2.c158 INLINE void transpose_vecs(__m256i vecs[DEGREE]) { in transpose_vecs()
161 __m256i ab_0145 = _mm256_unpacklo_epi32(vecs[0], vecs[1]); in transpose_vecs()
162 __m256i ab_2367 = _mm256_unpackhi_epi32(vecs[0], vecs[1]); in transpose_vecs()
163 __m256i cd_0145 = _mm256_unpacklo_epi32(vecs[2], vecs[3]); in transpose_vecs()
164 __m256i cd_2367 = _mm256_unpackhi_epi32(vecs[2], vecs[3]); in transpose_vecs()
165 __m256i ef_0145 = _mm256_unpacklo_epi32(vecs[4], vecs[5]); in transpose_vecs()
166 __m256i ef_2367 = _mm256_unpackhi_epi32(vecs[4], vecs[5]); in transpose_vecs()
167 __m256i gh_0145 = _mm256_unpacklo_epi32(vecs[6], vecs[7]); in transpose_vecs()
168 __m256i gh_2367 = _mm256_unpackhi_epi32(vecs[6], vecs[7]); in transpose_vecs()
182 vecs[0] = _mm256_permute2x128_si256(abcd_04, efgh_04, 0x20); in transpose_vecs()
[all …]
H A Dblake3_neon.c182 INLINE void transpose_vecs_128(uint32x4_t vecs[4]) { in transpose_vecs_128()
184 uint32x4x2_t rows01 = vtrnq_u32(vecs[0], vecs[1]); in transpose_vecs_128()
185 uint32x4x2_t rows23 = vtrnq_u32(vecs[2], vecs[3]); in transpose_vecs_128()
188 vecs[0] = in transpose_vecs_128()
190 vecs[1] = in transpose_vecs_128()
192 vecs[2] = in transpose_vecs_128()
194 vecs[3] = in transpose_vecs_128()
H A Dblake3_sse41.c392 INLINE void transpose_vecs(__m128i vecs[DEGREE]) { in transpose_vecs()
396 __m128i ab_01 = _mm_unpacklo_epi32(vecs[0], vecs[1]); in transpose_vecs()
397 __m128i ab_23 = _mm_unpackhi_epi32(vecs[0], vecs[1]); in transpose_vecs()
398 __m128i cd_01 = _mm_unpacklo_epi32(vecs[2], vecs[3]); in transpose_vecs()
399 __m128i cd_23 = _mm_unpackhi_epi32(vecs[2], vecs[3]); in transpose_vecs()
407 vecs[0] = abcd_0; in transpose_vecs()
408 vecs[1] = abcd_1; in transpose_vecs()
409 vecs[2] = abcd_2; in transpose_vecs()
410 vecs[3] = abcd_3; in transpose_vecs()
H A Dblake3_sse2.c398 INLINE void transpose_vecs(__m128i vecs[DEGREE]) { in transpose_vecs()
402 __m128i ab_01 = _mm_unpacklo_epi32(vecs[0], vecs[1]); in transpose_vecs()
403 __m128i ab_23 = _mm_unpackhi_epi32(vecs[0], vecs[1]); in transpose_vecs()
404 __m128i cd_01 = _mm_unpacklo_epi32(vecs[2], vecs[3]); in transpose_vecs()
405 __m128i cd_23 = _mm_unpackhi_epi32(vecs[2], vecs[3]); in transpose_vecs()
413 vecs[0] = abcd_0; in transpose_vecs()
414 vecs[1] = abcd_1; in transpose_vecs()
415 vecs[2] = abcd_2; in transpose_vecs()
416 vecs[3] = abcd_3; in transpose_vecs()
/freebsd/contrib/ntp/sntp/libevent/
H A Dbuffer_iocp.c256 struct evbuffer_iovec vecs[MAX_WSABUFS]; in evbuffer_launch_read_() local
274 vecs, MAX_WSABUFS, &chainp, 1); in evbuffer_launch_read_()
278 &vecs[i]); in evbuffer_launch_read_()
H A Devbuffer-internal.h326 struct evbuffer_iovec *vecs, int n_vecs, struct evbuffer_chain ***chainp,
H A Dbuffer.c2226 struct evbuffer_iovec *vecs, int n_vecs_avail, in evbuffer_read_setup_vecs_() argument
2252 vecs[i].iov_base = (void *)CHAIN_SPACE_PTR(chain); in evbuffer_read_setup_vecs_()
2253 vecs[i].iov_len = avail; in evbuffer_read_setup_vecs_()
2317 IOV_TYPE vecs[NUM_READ_IOVEC]; in evbuffer_read() local
2319 nvecs = evbuffer_read_setup_vecs_(buf, howmuch, vecs, in evbuffer_read()
2329 WSABUF_FROM_EVBUFFER_IOV(&vecs[i], &ev_vecs[i]); in evbuffer_read()
2336 if (WSARecv(fd, vecs, nvecs, &bytesRead, &flags, NULL, NULL)) { in evbuffer_read()
2347 n = readv(fd, vecs, nvecs); in evbuffer_read()
/freebsd/contrib/libevent/
H A Dbuffer_iocp.c256 struct evbuffer_iovec vecs[MAX_WSABUFS]; in evbuffer_launch_read_() local
274 vecs, MAX_WSABUFS, &chainp, 1); in evbuffer_launch_read_()
278 &vecs[i]); in evbuffer_launch_read_()
H A Devbuffer-internal.h326 struct evbuffer_iovec *vecs, int n_vecs, struct evbuffer_chain ***chainp,
H A Dbuffer.c2226 struct evbuffer_iovec *vecs, int n_vecs_avail, in evbuffer_read_setup_vecs_() argument
2252 vecs[i].iov_base = (void *)CHAIN_SPACE_PTR(chain); in evbuffer_read_setup_vecs_()
2253 vecs[i].iov_len = avail; in evbuffer_read_setup_vecs_()
2317 IOV_TYPE vecs[NUM_READ_IOVEC]; in evbuffer_read() local
2319 nvecs = evbuffer_read_setup_vecs_(buf, howmuch, vecs, in evbuffer_read()
2329 WSABUF_FROM_EVBUFFER_IOV(&vecs[i], &ev_vecs[i]); in evbuffer_read()
2336 if (WSARecv(fd, vecs, nvecs, &bytesRead, &flags, NULL, NULL)) { in evbuffer_read()
2347 n = readv(fd, vecs, nvecs); in evbuffer_read()
/freebsd/sys/contrib/device-tree/src/mips/loongson/
H A Dloongson64c_4core_ls7a.dts34 loongson,msi-num-vecs = <64>;
H A Dloongson64g_4core_ls7a.dts39 loongson,msi-num-vecs = <192>;
/freebsd/sys/contrib/device-tree/src/loongarch/
H A Dloongson-2k2000.dtsi164 loongson,msi-num-vecs = <192>;