Home
last modified time | relevance | path

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

12

/f-stack/freebsd/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.
/f-stack/freebsd/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 …]
/f-stack/freebsd/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 …]
/f-stack/freebsd/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); \
/f-stack/freebsd/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 …]
/f-stack/freebsd/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>
/f-stack/freebsd/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_avx512bw.c96 #define XOR(r...) \ macro
116 #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_scalar.c93 #define XOR(src, acc) acc.e ^= src.e macro
H A Dvdev_raidz_math_powerpc_altivec_common.h207 #define XOR(r...) \ macro
/f-stack/dpdk/devtools/
H A Dwords-case.txt76 XOR
/f-stack/dpdk/doc/guides/prog_guide/
H A Dlink_bonding_poll_mode_drv_lib.rst66 * **Balance XOR (Mode 2):**
70 Balance XOR (Mode 2)
270 the device is in balance XOR mode.
304 Balance XOR Transmit Policies
308 Balance XOR mode. Layer 2, Layer 2+3, Layer 3+4.
311 transmission policy for Balance XOR bonding mode. It uses a simple XOR
/f-stack/dpdk/doc/guides/nics/
H A Docteontx2.rst172 - ``RSS tag as XOR`` (default ``0``)
186 For example to select the legacy mode(RSS tag adder as XOR)::
/f-stack/dpdk/doc/guides/sample_app_ug/
H A Dskeleton.rst275 using the an XOR on the port number::
H A Ddist_app.rst84 the distributor, doing a simple XOR operation on the input port mbuf field
H A Dflow_classify.rst529 using the an XOR on the port number::
/f-stack/freebsd/contrib/device-tree/Bindings/
H A Dexample-schema.yaml38 # More complicated schema can use oneOf (XOR), anyOf (OR), or allOf (AND)
/f-stack/freebsd/contrib/device-tree/Bindings/mmc/
H A Dmmc-controller.yaml60 # latter case. We choose to use the XOR logic for GPIO CD and WP
/f-stack/freebsd/contrib/device-tree/Bindings/arm/marvell/
H A Dcp110-system-controller.txt55 - 1 14 PCIe / XOR
/f-stack/dpdk/drivers/common/dpaax/caamflib/desc/
H A Dsdap.h288 MATHB(p, MATH1, XOR, PDCP_NULL_INT_MAC_I_VAL, NONE, 4, IMMED2); in pdcp_sdap_insert_enc_only_op()

12