Home
last modified time | relevance | path

Searched refs:iv0 (Results 1 – 25 of 26) sorted by relevance

12

/netbsd-src/external/gpl3/gcc/dist/gcc/
H A Dloop-iv.cc511 iv_add (class rtx_iv *iv0, class rtx_iv *iv1, enum rtx_code op) in iv_add() argument
517 if (iv0->extend == IV_UNKNOWN_EXTEND in iv_add()
518 && iv0->mode == iv0->extend_mode in iv_add()
519 && iv0->step == const0_rtx in iv_add()
520 && GET_MODE_SIZE (iv0->extend_mode) < GET_MODE_SIZE (iv1->extend_mode)) in iv_add()
522 iv0->extend_mode = iv1->extend_mode; in iv_add()
523 iv0->base = simplify_gen_unary (ZERO_EXTEND, iv0->extend_mode, in iv_add()
524 iv0->base, iv0->mode); in iv_add()
529 && GET_MODE_SIZE (iv1->extend_mode) < GET_MODE_SIZE (iv0->extend_mode)) in iv_add()
531 iv1->extend_mode = iv0->extend_mode; in iv_add()
[all …]
H A Dtree-ssa-loop-niter.cc1162 number_of_iterations_lt_to_ne (tree type, affine_iv *iv0, affine_iv *iv1, in number_of_iterations_lt_to_ne() argument
1200 (iv0->no_overflow && integer_nonzerop (iv0->step)) in number_of_iterations_lt_to_ne()
1203 if (integer_nonzerop (iv0->step)) in number_of_iterations_lt_to_ne()
1221 iv0->base, in number_of_iterations_lt_to_ne()
1225 iv0->base, in number_of_iterations_lt_to_ne()
1239 iv0->base, bound); in number_of_iterations_lt_to_ne()
1247 fold_build_pointer_plus (iv0->base, in number_of_iterations_lt_to_ne()
1254 iv0->base, tmod), in number_of_iterations_lt_to_ne()
1281 assert_no_overflow_lt (tree type, affine_iv *iv0, affine_iv *iv1, in assert_no_overflow_lt() argument
1287 if (integer_nonzerop (iv0->step)) in assert_no_overflow_lt()
[all …]
H A Dpredict.cc1512 affine_iv iv0, iv1; in is_comparison_with_loop_invariant_p() local
1539 if (!simple_iv (loop, loop_containing_stmt (stmt), op0, &iv0, true)) in is_comparison_with_loop_invariant_p()
1543 if (TREE_CODE (iv0.step) != INTEGER_CST in is_comparison_with_loop_invariant_p()
1546 if ((integer_zerop (iv0.step) && integer_zerop (iv1.step)) in is_comparison_with_loop_invariant_p()
1547 || (!integer_zerop (iv0.step) && !integer_zerop (iv1.step))) in is_comparison_with_loop_invariant_p()
1550 if (integer_zerop (iv0.step)) in is_comparison_with_loop_invariant_p()
1554 bound = iv0.base; in is_comparison_with_loop_invariant_p()
1564 base = iv0.base; in is_comparison_with_loop_invariant_p()
1565 if (tree_fits_shwi_p (iv0.step)) in is_comparison_with_loop_invariant_p()
1566 step = iv0.step; in is_comparison_with_loop_invariant_p()
H A Dtree-ssa-loop-ivopts.cc1703 struct iv *iv0 = &const_iv, *iv1 = &const_iv; in extract_cond_operands() local
1722 iv0 = get_iv (data, *op0); in extract_cond_operands()
1727 if (iv0 && iv1 && !integer_zerop (iv0->step) && !integer_zerop (iv1->step)) in extract_cond_operands()
1734 if ((!iv0 || integer_zerop (iv0->step)) in extract_cond_operands()
1739 if (!iv0 || integer_zerop (iv0->step)) in extract_cond_operands()
1742 std::swap (iv0, iv1); in extract_cond_operands()
1748 else if (!integer_zerop (iv0->step) && integer_zerop (iv1->step)) in extract_cond_operands()
1755 *iv_var = iv0; in extract_cond_operands()
/netbsd-src/external/gpl3/gcc.old/dist/gcc/
H A Dloop-iv.c511 iv_add (class rtx_iv *iv0, class rtx_iv *iv1, enum rtx_code op) in iv_add() argument
517 if (iv0->extend == IV_UNKNOWN_EXTEND in iv_add()
518 && iv0->mode == iv0->extend_mode in iv_add()
519 && iv0->step == const0_rtx in iv_add()
520 && GET_MODE_SIZE (iv0->extend_mode) < GET_MODE_SIZE (iv1->extend_mode)) in iv_add()
522 iv0->extend_mode = iv1->extend_mode; in iv_add()
523 iv0->base = simplify_gen_unary (ZERO_EXTEND, iv0->extend_mode, in iv_add()
524 iv0->base, iv0->mode); in iv_add()
529 && GET_MODE_SIZE (iv1->extend_mode) < GET_MODE_SIZE (iv0->extend_mode)) in iv_add()
531 iv1->extend_mode = iv0->extend_mode; in iv_add()
[all …]
H A Dtree-ssa-loop-niter.c1150 number_of_iterations_lt_to_ne (tree type, affine_iv *iv0, affine_iv *iv1, in number_of_iterations_lt_to_ne() argument
1188 (iv0->no_overflow && integer_nonzerop (iv0->step)) in number_of_iterations_lt_to_ne()
1191 if (integer_nonzerop (iv0->step)) in number_of_iterations_lt_to_ne()
1209 iv0->base, in number_of_iterations_lt_to_ne()
1213 iv0->base, in number_of_iterations_lt_to_ne()
1227 iv0->base, bound); in number_of_iterations_lt_to_ne()
1235 fold_build_pointer_plus (iv0->base, in number_of_iterations_lt_to_ne()
1242 iv0->base, tmod), in number_of_iterations_lt_to_ne()
1269 assert_no_overflow_lt (tree type, affine_iv *iv0, affine_iv *iv1, in assert_no_overflow_lt() argument
1275 if (integer_nonzerop (iv0->step)) in assert_no_overflow_lt()
[all …]
H A Dpredict.c1474 affine_iv iv0, iv1; in is_comparison_with_loop_invariant_p() local
1501 if (!simple_iv (loop, loop_containing_stmt (stmt), op0, &iv0, true)) in is_comparison_with_loop_invariant_p()
1505 if (TREE_CODE (iv0.step) != INTEGER_CST in is_comparison_with_loop_invariant_p()
1508 if ((integer_zerop (iv0.step) && integer_zerop (iv1.step)) in is_comparison_with_loop_invariant_p()
1509 || (!integer_zerop (iv0.step) && !integer_zerop (iv1.step))) in is_comparison_with_loop_invariant_p()
1512 if (integer_zerop (iv0.step)) in is_comparison_with_loop_invariant_p()
1516 bound = iv0.base; in is_comparison_with_loop_invariant_p()
1526 base = iv0.base; in is_comparison_with_loop_invariant_p()
1527 if (tree_fits_shwi_p (iv0.step)) in is_comparison_with_loop_invariant_p()
1528 step = iv0.step; in is_comparison_with_loop_invariant_p()
H A Dtree-ssa-loop-ivopts.c1704 struct iv *iv0 = &const_iv, *iv1 = &const_iv; in extract_cond_operands() local
1723 iv0 = get_iv (data, *op0); in extract_cond_operands()
1728 if (iv0 && iv1 && !integer_zerop (iv0->step) && !integer_zerop (iv1->step)) in extract_cond_operands()
1735 if ((!iv0 || integer_zerop (iv0->step)) in extract_cond_operands()
1740 if (!iv0 || integer_zerop (iv0->step)) in extract_cond_operands()
1743 std::swap (iv0, iv1); in extract_cond_operands()
1749 else if (!integer_zerop (iv0->step) && integer_zerop (iv1->step)) in extract_cond_operands()
1756 *iv_var = iv0; in extract_cond_operands()
/netbsd-src/crypto/external/bsd/openssl/dist/crypto/aes/asm/
H A Daesv8-armx.pl2231 my ($iv0,$iv1,$iv2,$iv3,$iv4)=("v6.16b","v8.16b","v9.16b","v10.16b","v11.16b");
2265 vld1.8 {$iv0},[$ivp]
2270 aese $iv0,$dat
2271 aesmc $iv0,$iv0
2274 aese $iv0,$dat1
2275 aesmc $iv0,$iv0
2279 aese $iv0,$dat
2280 aesmc $iv0,$iv0
2282 aese $iv0,$dat1
2283 veor $iv0,$iv0,$dat
[all …]
H A Daesfx-sparcv9.pl394 my ($iv0,$iv1,$r0hi,$r0lo,$rlhi,$rllo,$in0,$in1,$intail,$outhead,$fshift)
654 fmovd %f0, $iv0
691 fxor $iv0, $rlhi, %f6 ! ivec^round[last]
693 fmovd $in0, $iv0
725 st $iv0, [$ivp + 0] ! output ivec
726 st $iv0#lo, [$ivp + 4]
820 fxor $iv0, $rlhi, %f6 ! ivec^round[last]
822 fmovd $in0, $iv0
850 st $iv0, [$ivp + 0] ! output ivec
851 st $iv0#lo, [$ivp + 4]
H A Daes-s390x.pl1390 my $key="%r5"; my $iv0="%r5";
1468 lg $iv0,0($ivp) # load ivec
1517 stg $iv0,0($s2)
1546 stg $iv0,0($s2)
/netbsd-src/sys/crypto/aes/
H A Daes_selftest.c212 uint8_t iv0[16], iv[16]; in aes_selftest_encdec_cbc() local
218 iv0[i] = 0x20 ^ i; in aes_selftest_encdec_cbc()
227 memcpy(iv, iv0, 16); in aes_selftest_encdec_cbc()
233 memcpy(iv, iv0, 16); in aes_selftest_encdec_cbc()
241 memcpy(iv, iv0, 16); in aes_selftest_encdec_cbc()
250 memcpy(iv, iv0, 16); in aes_selftest_encdec_cbc()
342 uint8_t iv0[16], iv[16]; in aes_selftest_encdec_xts() local
358 impl->ai_enc(&enc, blkno_buf, iv0, aes_nrounds[i]); in aes_selftest_encdec_xts()
365 memcpy(iv, iv0, 16); in aes_selftest_encdec_xts()
371 memcpy(iv, iv0, 16); in aes_selftest_encdec_xts()
[all …]
H A Daes_bear.c223 uint32_t cv0, cv1, cv2, cv3, iv0, iv1, iv2, iv3; in aesbear_cbc_dec() local
235 iv0 = le32dec(iv + 4*0); in aesbear_cbc_dec()
334 le32enc(out + 4*0, q[2*0] ^ iv0); in aesbear_cbc_dec()
/netbsd-src/crypto/dist/ipsec-tools/src/racoon/
H A Deaytest.c595 vchar_t *iv0, in ciphertest_1() argument
616 memcpy(iv->v, iv0->v, iv_length); in ciphertest_1()
625 memcpy(iv->v, iv0->v, iv_length); in ciphertest_1()
655 vchar_t iv0; local
664 iv0.v = str2val("26b68c90 9467b4ab 7ec29fa0 0b696b55", 16, &iv0.l);
669 &iv0, 8,
676 &iv0, 8,
683 &iv0, 16,
690 &iv0, 8,
697 &iv0, 8,
[all …]
/netbsd-src/crypto/external/bsd/openssl.old/dist/crypto/aes/asm/
H A Daesfx-sparcv9.pl392 my ($iv0,$iv1,$r0hi,$r0lo,$rlhi,$rllo,$in0,$in1,$intail,$outhead,$fshift)
652 fmovd %f0, $iv0
689 fxor $iv0, $rlhi, %f6 ! ivec^round[last]
691 fmovd $in0, $iv0
723 st $iv0, [$ivp + 0] ! output ivec
724 st $iv0#lo, [$ivp + 4]
818 fxor $iv0, $rlhi, %f6 ! ivec^round[last]
820 fmovd $in0, $iv0
848 st $iv0, [$ivp + 0] ! output ivec
849 st $iv0#lo, [$ivp + 4]
H A Daes-s390x.pl1388 my $key="%r5"; my $iv0="%r5";
1466 lg $iv0,0($ivp) # load ivec
1515 stg $iv0,0($s2)
1544 stg $iv0,0($s2)
/netbsd-src/sys/crypto/aes/arch/x86/
H A Daes_ssse3_subr.c101 __m128i iv0, cv, b; in aes_ssse3_cbc_dec() local
106 iv0 = loadblock(iv); in aes_ssse3_cbc_dec()
117 storeblock(out, b ^ iv0); in aes_ssse3_cbc_dec()
H A Daes_via.c417 uint8_t iv0[16] __aligned(16); in aesvia_cbc_dec() local
421 memcpy(iv0, iv, 16); in aesvia_cbc_dec()
434 xor128(tmp, tmp, iv0); in aesvia_cbc_dec()
/netbsd-src/sys/crypto/aes/arch/arm/
H A Daes_neon_subr.c104 uint8x16_t iv0, cv, b; in aes_neon_cbc_dec() local
109 iv0 = loadblock(iv); in aes_neon_cbc_dec()
139 out: storeblock(out, b ^ iv0); in aes_neon_cbc_dec()
/netbsd-src/sys/external/isc/libsodium/dist/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-compress-avx2.h128 const __m256i iv0 = a; \
136 a = XOR(a, iv0); \
/netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/subdev/pmu/fuc/
H A Dkernel.fuc528 mov $iv0 $r1
/netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/engine/gr/fuc/
H A Dgpc.fuc139 mov $iv0 $r1
H A Dhub.fuc85 mov $iv0 $r1
/netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/engine/sec/fuc/
H A Dg98.fuc0s104 mov $iv0 $r1
/netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/engine/ce/fuc/
H A Dcom.fuc142 mov $iv0 $r1

12