Home
last modified time | relevance | path

Searched refs:XOR (Results 1 – 25 of 152) sorted by relevance

1234567

/freebsd-13.1/contrib/unbound/compat/
H A Dchacha_private.h41 #define XOR(v,w) ((v) ^ (w)) macro
49 c = PLUS(c,d); b = ROTATE(XOR(b,c), 7);
167 x0 = XOR(x0,U8TO32_LITTLE(m + 0)); in chacha_encrypt_bytes()
168 x1 = XOR(x1,U8TO32_LITTLE(m + 4)); in chacha_encrypt_bytes()
169 x2 = XOR(x2,U8TO32_LITTLE(m + 8)); in chacha_encrypt_bytes()
170 x3 = XOR(x3,U8TO32_LITTLE(m + 12)); in chacha_encrypt_bytes()
171 x4 = XOR(x4,U8TO32_LITTLE(m + 16)); in chacha_encrypt_bytes()
172 x5 = XOR(x5,U8TO32_LITTLE(m + 20)); in chacha_encrypt_bytes()
173 x6 = XOR(x6,U8TO32_LITTLE(m + 24)); in chacha_encrypt_bytes()
174 x7 = XOR(x7,U8TO32_LITTLE(m + 28)); in chacha_encrypt_bytes()
[all …]
/freebsd-13.1/crypto/openssh/openbsd-compat/
H A Dchacha_private.h41 #define XOR(v,w) ((v) ^ (w)) macro
49 c = PLUS(c,d); b = ROTATE(XOR(b,c), 7);
167 x0 = XOR(x0,U8TO32_LITTLE(m + 0)); in chacha_encrypt_bytes()
168 x1 = XOR(x1,U8TO32_LITTLE(m + 4)); in chacha_encrypt_bytes()
169 x2 = XOR(x2,U8TO32_LITTLE(m + 8)); in chacha_encrypt_bytes()
170 x3 = XOR(x3,U8TO32_LITTLE(m + 12)); in chacha_encrypt_bytes()
171 x4 = XOR(x4,U8TO32_LITTLE(m + 16)); in chacha_encrypt_bytes()
172 x5 = XOR(x5,U8TO32_LITTLE(m + 20)); in chacha_encrypt_bytes()
173 x6 = XOR(x6,U8TO32_LITTLE(m + 24)); in chacha_encrypt_bytes()
174 x7 = XOR(x7,U8TO32_LITTLE(m + 28)); in chacha_encrypt_bytes()
[all …]
/freebsd-13.1/crypto/openssh/
H A Dchacha.c42 #define XOR(v,w) ((v) ^ (w)) macro
50 c = PLUS(c,d); b = ROTATE(XOR(b,c), 7);
167 x0 = XOR(x0,U8TO32_LITTLE(m + 0)); in chacha_encrypt_bytes()
168 x1 = XOR(x1,U8TO32_LITTLE(m + 4)); in chacha_encrypt_bytes()
169 x2 = XOR(x2,U8TO32_LITTLE(m + 8)); in chacha_encrypt_bytes()
170 x3 = XOR(x3,U8TO32_LITTLE(m + 12)); in chacha_encrypt_bytes()
171 x4 = XOR(x4,U8TO32_LITTLE(m + 16)); in chacha_encrypt_bytes()
172 x5 = XOR(x5,U8TO32_LITTLE(m + 20)); in chacha_encrypt_bytes()
173 x6 = XOR(x6,U8TO32_LITTLE(m + 24)); in chacha_encrypt_bytes()
174 x7 = XOR(x7,U8TO32_LITTLE(m + 28)); in chacha_encrypt_bytes()
[all …]
/freebsd-13.1/sys/crypto/chacha20/
H A Dchacha.c46 #define XOR(v,w) ((v) ^ (w)) macro
54 c = PLUS(c,d); b = ROTATE(XOR(b,c), 7);
194 x0 = XOR(x0,U8TO32_LITTLE(m + 0)); in chacha_encrypt_bytes()
195 x1 = XOR(x1,U8TO32_LITTLE(m + 4)); in chacha_encrypt_bytes()
196 x2 = XOR(x2,U8TO32_LITTLE(m + 8)); in chacha_encrypt_bytes()
197 x3 = XOR(x3,U8TO32_LITTLE(m + 12)); in chacha_encrypt_bytes()
198 x4 = XOR(x4,U8TO32_LITTLE(m + 16)); in chacha_encrypt_bytes()
199 x5 = XOR(x5,U8TO32_LITTLE(m + 20)); in chacha_encrypt_bytes()
200 x6 = XOR(x6,U8TO32_LITTLE(m + 24)); in chacha_encrypt_bytes()
201 x7 = XOR(x7,U8TO32_LITTLE(m + 28)); in chacha_encrypt_bytes()
[all …]
/freebsd-13.1/sys/contrib/device-tree/Bindings/dma/
H A Dmv-xor.txt1 * Marvell XOR engines
10 registers for the XOR engine.
13 The DT node must also contains sub-nodes for each XOR channel that the
14 XOR engine has. Those sub-nodes have the following required
16 - interrupts: interrupt of the XOR channel
20 - dmacap,memcpy to indicate that the XOR channel is capable of memcpy operations
21 - dmacap,memset to indicate that the XOR channel is capable of memset operations
22 - dmacap,xor to indicate that the XOR channel is capable of xor operations
23 - dmacap,interrupt to indicate that the XOR channel is capable of
H A Dmv-xor-v2.txt1 * Marvell XOR v2 engines
14 - clocks: Optional reference to the clocks used by the XOR engine.
/freebsd-13.1/sys/contrib/libsodium/src/libsodium/crypto_stream/chacha20/ref/
H A Dchacha20_ref.c31 #define XOR(v, w) ((v) ^ (w)) macro
37 d = ROTATE(XOR(d, a), 16); \
39 b = ROTATE(XOR(b, c), 12); \
41 d = ROTATE(XOR(d, a), 8); \
43 b = ROTATE(XOR(b, c), 7);
168 x0 = XOR(x0, LOAD32_LE(m + 0)); in chacha20_encrypt_bytes()
169 x1 = XOR(x1, LOAD32_LE(m + 4)); in chacha20_encrypt_bytes()
170 x2 = XOR(x2, LOAD32_LE(m + 8)); in chacha20_encrypt_bytes()
171 x3 = XOR(x3, LOAD32_LE(m + 12)); in chacha20_encrypt_bytes()
172 x4 = XOR(x4, LOAD32_LE(m + 16)); in chacha20_encrypt_bytes()
[all …]
/freebsd-13.1/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-compress-avx2.h33 #define XOR(a, b) _mm256_xor_si256(a, b) macro
46 d = XOR(d, a); \
49 b = XOR(b, c); \
57 d = XOR(d, a); \
60 b = XOR(b, c); \
129 XOR(LOAD(&blake2b_IV[4]), _mm256_set_epi64x(f1, f0, t1, t0)); \
131 a = XOR(a, c); \
132 b = XOR(b, d); \
133 a = XOR(a, iv0); \
134 b = XOR(b, iv1); \
/freebsd-13.1/sys/contrib/device-tree/Bindings/clock/
H A Dmvebu-gated-clock.txt45 22 xor0 XOR DMA 0
46 23 xor1 XOR DMA 0
75 22 xor0 XOR 0
78 28 xor1 XOR 1
92 22 xor0 XOR 0
93 28 xor1 XOR 1
115 22 xor0 XOR DMA 0
118 28 xor1 XOR DMA 1
130 22 xor0 XOR DMA 0
150 23 xor0 XOR DMA 0
[all …]
/freebsd-13.1/contrib/llvm-project/llvm/lib/Target/Lanai/
H A DLanaiAluCode.h29 XOR = 0x06, enumerator
90 case XOR: in lanaiAluCodeToString()
111 .Case("xor", XOR) in stringToLanaiAluCode()
132 case ISD::XOR: in isdToLanaiAluCode()
133 return AluCode::XOR; in isdToLanaiAluCode()
/freebsd-13.1/sys/contrib/device-tree/Bindings/powerpc/4xx/
H A Dppc440spe-adma.txt1 PPC440SPe DMA/XOR (DMA Controller and XOR Accelerator)
4 are specified hereby. These are I2O/DMA, DMA and XOR nodes
60 iii) XOR Accelerator node
66 - interrupts : <interrupt mapping for XOR interrupt source>
/freebsd-13.1/sys/contrib/openzfs/module/zfs/
H A Dvdev_raidz_math_avx512f.c102 #define XOR(r...) \ macro
121 #define ZERO(r...) XOR(r, r)
234 if (x & 0x02) { XOR(in, acc); } \
236 if (x & 0x04) { XOR(in, acc); } \
238 if (x & 0x08) { XOR(in, acc); } \
240 if (x & 0x10) { XOR(in, acc); } \
242 if (x & 0x20) { XOR(in, acc); } \
244 if (x & 0x40) { XOR(in, acc); } \
245 if (x & 0x80) { MUL2(in); XOR(in, acc); } \
H A Dvdev_raidz_math_impl.h302 XOR(D, T); \
310 XOR(D, T); \
325 XOR(D, T); \
878 XOR(REC_PQ_Y, REC_PQ_X); in raidz_rec_pq_abd()
882 XOR(REC_PQ_T, REC_PQ_X); in raidz_rec_pq_abd()
1038 XOR(REC_PR_Y, REC_PR_X); in raidz_rec_pr_abd()
1042 XOR(REC_PR_T, REC_PR_X); in raidz_rec_pr_abd()
1202 XOR(REC_QR_Y, REC_QR_X); /* X = R ^ X */ in raidz_rec_qr_abd()
1208 XOR(REC_QR_Y, REC_QR_T); /* X = R ^ X */ in raidz_rec_qr_abd()
1380 XOR(REC_PQR_Y, REC_PQR_X); in raidz_rec_pqr_abd()
[all …]
H A Dvdev_raidz_math_sse2.c88 #define XOR(r...) \ macro
110 #define ZERO(r...) XOR(r, r)
249 if (x & 0x02) { XOR(in, acc); } \
251 if (x & 0x04) { XOR(in, acc); } \
253 if (x & 0x08) { XOR(in, acc); } \
255 if (x & 0x10) { XOR(in, acc); } \
257 if (x & 0x20) { XOR(in, acc); } \
259 if (x & 0x40) { XOR(in, acc); } \
260 if (x & 0x80) { MUL2(in); XOR(in, acc); } \
H A Dvdev_raidz_math_ssse3.c94 #define XOR(r...) \ macro
114 #define ZERO(r...) XOR(r, r)
H A Dvdev_raidz_math_avx2.c93 #define XOR(r...) \ macro
113 #define ZERO(r...) XOR(r, r)
H A Dvdev_raidz_math_avx512bw.c96 #define XOR(r...) \ macro
116 #define ZERO(r...) XOR(r, r)
H A Dvdev_raidz_math_scalar.c93 #define XOR(src, acc) acc.e ^= src.e macro
/freebsd-13.1/contrib/llvm-project/llvm/lib/Target/Mips/
H A DMipsCondMov.td201 defm : MovzPats1<GPR32, GPR32, MOVZ_I_I, XOR>, INSN_MIPS4_32_NOT_32R6_64R6;
210 defm : MovzPats1<GPR32, GPR64, MOVZ_I_I64, XOR>,
223 defm : MovnPats<GPR32, GPR32, MOVN_I_I, XOR>, INSN_MIPS4_32_NOT_32R6_64R6;
225 defm : MovnPats<GPR32, GPR64, MOVN_I_I64, XOR>, INSN_MIPS4_32_NOT_32R6_64R6,
234 defm : MovzPats1<GPR32, FGR32, MOVZ_I_S, XOR>, INSN_MIPS4_32_NOT_32R6_64R6;
235 defm : MovnPats<GPR32, FGR32, MOVN_I_S, XOR>, INSN_MIPS4_32_NOT_32R6_64R6;
246 defm : MovzPats1<GPR32, AFGR64, MOVZ_I_D32, XOR>, INSN_MIPS4_32_NOT_32R6_64R6,
248 defm : MovnPats<GPR32, AFGR64, MOVN_I_D32, XOR>, INSN_MIPS4_32_NOT_32R6_64R6,
255 defm : MovzPats1<GPR32, FGR64, MOVZ_I_D64, XOR>, INSN_MIPS4_32_NOT_32R6_64R6,
259 defm : MovnPats<GPR32, FGR64, MOVN_I_D64, XOR>, INSN_MIPS4_32_NOT_32R6_64R6,
/freebsd-13.1/contrib/llvm-project/llvm/lib/Target/PowerPC/
H A DPPCExpandAtomicPseudoInsts.cpp56 const MCInstrDesc &XOR = TII->get(PPC::XOR8); in PairedCopy() local
59 BuildMI(MBB, MBBI, DL, XOR, Dest0).addReg(Dest0).addReg(Dest1); in PairedCopy()
60 BuildMI(MBB, MBBI, DL, XOR, Dest1).addReg(Dest0).addReg(Dest1); in PairedCopy()
61 BuildMI(MBB, MBBI, DL, XOR, Dest0).addReg(Dest0).addReg(Dest1); in PairedCopy()
H A DPPCISelDAGToDAG.cpp2770 case ISD::XOR: in Select()
3897 case ISD::XOR: { in tryIntCompareInGPR()
5276 case ISD::XOR: { in Select()
5933 XOR = XOR.getOperand(0); in combineToCMPB()
5934 if (XOR.getOpcode() != ISD::XOR) in combineToCMPB()
5937 LHS = XOR.getOperand(0); in combineToCMPB()
5938 RHS = XOR.getOperand(1); in combineToCMPB()
5951 XOR = XOR.getOperand(0); in combineToCMPB()
5952 if (XOR.getOpcode() != ISD::XOR) in combineToCMPB()
5955 LHS = XOR.getOperand(0); in combineToCMPB()
[all …]
/freebsd-13.1/contrib/llvm-project/llvm/lib/Target/AArch64/
H A DAArch64TargetTransformInfo.cpp1388 case ISD::XOR: in getArithmeticInstrCost()
1944 case ISD::XOR: in getArithmeticReductionCostSVE()
1999 {ISD::XOR, MVT::v8i8, 15}, in getArithmeticReductionCost()
2000 {ISD::XOR, MVT::v16i8, 17}, in getArithmeticReductionCost()
2001 {ISD::XOR, MVT::v4i16, 7}, in getArithmeticReductionCost()
2002 {ISD::XOR, MVT::v8i16, 9}, in getArithmeticReductionCost()
2003 {ISD::XOR, MVT::v2i32, 3}, in getArithmeticReductionCost()
2004 {ISD::XOR, MVT::v4i32, 5}, in getArithmeticReductionCost()
2005 {ISD::XOR, MVT::v2i64, 3}, in getArithmeticReductionCost()
2021 case ISD::XOR: in getArithmeticReductionCost()
/freebsd-13.1/contrib/llvm-project/llvm/lib/TableGen/
H A DTGLexer.h55 XConcat, XADD, XSUB, XMUL, XNOT, XAND, XOR, XXOR, XSRA, XSRL, XSHL, enumerator
/freebsd-13.1/contrib/llvm-project/llvm/lib/Target/M68k/
H A DM68kISelLowering.cpp1693 case ISD::XOR: { in EmitTest()
1749 case ISD::XOR: in EmitTest()
1763 case ISD::XOR: in EmitTest()
1764 Opcode = M68kISD::XOR; in EmitTest()
1779 case M68kISD::XOR: in EmitTest()
1812 case ISD::XOR: in EmitTest()
1813 ConvertedOp = M68kISD::XOR; in EmitTest()
1951 SDValue Xor = DAG.getNode(ISD::XOR, DL, MVT::i1, Op0, Op1); in LowerSETCC()
1998 Opc == M68kISD::OR || Opc == M68kISD::XOR || Opc == M68kISD::AND)) in isM68kLogicalCmp()
2233 if (Op.getOpcode() != ISD::XOR) in isXor1OfSetCC()
[all …]
/freebsd-13.1/contrib/llvm-project/llvm/lib/Target/X86/
H A DX86ISelDAGToDAG.cpp591 case X86ISD::XOR: in IsProfitableToFold()
597 case ISD::XOR: { in IsProfitableToFold()
1142 case X86ISD::FXOR: Opc = ISD::XOR; break; in PreprocessISelDAG()
3153 case X86ISD::XOR: in foldLoadStoreIntoMemOperand()
3229 case X86ISD::XOR: { in foldLoadStoreIntoMemOperand()
3249 case X86ISD::XOR: in foldLoadStoreIntoMemOperand()
3270 case X86ISD::XOR: in foldLoadStoreIntoMemOperand()
3296 case X86ISD::XOR: in foldLoadStoreIntoMemOperand()
3441 if (Mask.getOpcode() != ISD::XOR || !checkOneUse(Mask)) in matchBitExtract()
4235 case ISD::XOR: Imm ^= TernlogMagicA; break; in tryVPTERNLOG()
[all …]

1234567