| /src/sys/external/isc/libsodium/dist/src/libsodium/crypto_pwhash/argon2/ |
| blamka-round-avx512f.h | 17 #define G1_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \
19 A0 = muladd(A0, B0); \
22 D0 = _mm512_xor_si512(D0, A0); \
38 #define G2_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \
40 A0 = muladd(A0, B0); \
43 D0 = _mm512_xor_si512(D0, A0); \
59 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \
71 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1)
[all...] |
| blamka-round-avx2.h | 12 #define G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
14 __m256i ml = _mm256_mul_epu32(A0, B0); \
16 A0 = _mm256_add_epi64(A0, _mm256_add_epi64(B0, ml)); \
17 D0 = _mm256_xor_si256(D0, A0); \
41 #define G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \
43 __m256i ml = _mm256_mul_epu32(A0, B0); \
45 A0 = _mm256_add_epi64(A0, _mm256_add_epi64(B0, ml)); \
46 D0 = _mm256_xor_si256(D0, A0); \
[all...] |
| blamka-round-ssse3.h | 31 #define G1(A0, B0, C0, D0, A1, B1, C1, D1) \
33 A0 = fBlaMka(A0, B0); \
36 D0 = _mm_xor_si128(D0, A0); \
52 #define G2(A0, B0, C0, D0, A1, B1, C1, D1) \
54 A0 = fBlaMka(A0, B0); \
57 D0 = _mm_xor_si128(D0, A0); \
73 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \
90 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1)
[all...] |
| /src/sys/arch/m68k/include/ |
| reg.h | 48 int r_regs[16]; /* D0-D7/A0-A7 */
76 #define A0 (8)
96 #define R1 A0
|
| /src/sys/arch/m68k/m68k/ |
| m68k_machdep.c | 108 tf->tf_regs[A0] = 0;
|
| m68k_syscall.c | 239 * stubs properly handle returning pointers in %a0
249 * %a0 is preserved across system calls...
252 frame->f_regs[A0] = rval[0];
372 * %a0 is preserved across system calls...
375 frame->f_regs[A0] = rval[0];
|
| sig_machdep.c | 212 gr[_REG_A0] = frame->f_regs[A0];
352 frame->f_regs[A0] = gr[_REG_A0];
|
| /src/sys/external/bsd/drm2/dist/drm/amd/display/include/ |
| set_mode_types.h | 66 uint8_t A0:1;
|
| /src/sys/external/bsd/drm2/dist/drm/amd/display/modules/color/ |
| color_gamma.h | 47 unsigned int coeffFromUser :1; //coeff. A0-A3 from user is in use
48 unsigned int coeffFromEdid :1; //coeff. A0-A3 from edid is in use
64 int A0[3];
89 struct fixed31_32 a0; member in struct:translate_from_linear_space_args
|
| /src/sys/arch/m68k/060sp/dist/ |
| changes | 51 was A0 or A1, the address register was not being updated as a result
|
| isp.s | 292 set EXC_A0, EXC_AREGS+(0*4) # offset of a0
411 movm.l &0x3fff,EXC_DREGS(%a6) # store d0-d7/a0-a5
417 mov.l %usp,%a0 # fetch user stack pointer
418 mov.l %a0,EXC_A7(%a6) # store a7
421 lea 0xc(%a6),%a0
422 mov.l %a0,EXC_A7(%a6) # store corrected sp
436 mov.l EXC_EXTWPTR(%a6),%a0 # fetch instruction addr
559 mov.l EXC_EXTWPTR(%a6),%a0 # fetch instruction addr
594 mov.l EXC_A7(%a6),%a0 # fetch user stack pointer
595 mov.l %a0,%usp # restore i
[all...] |
| /src/sys/arch/m68k/fpsp/ |
| fpsp.h | 46 * movem.l d0-d1/a0-a1,USER_DA(a6)
76 * movem.l USER_DA(a6),d0-d1/a0-a1
95 * The registers d0, d1, a0, a1 and fp0-fp3 are always saved and variable
108 USER_DA equ LV+0 ;save space for D0-D1,A0-A1
111 USER_A0 equ LV+8 ;saved user A0
|
| l_fpsp.h | 57 * movem.l d0-d1/a0-a1,USER_DA(a6)
84 * movem.l USER_DA(a6),d0-d1/a0-a1
90 * Many 68K C compilers treat a0/a1/d0/d1/fp0/fp1 as scratch so
120 USER_DA equ LV+0 ;save space for D0-D1,A0-A1
123 USER_A0 equ LV+8 ;saved user A0
|
| /src/sys/arch/mac68k/mac68k/ |
| macromasm.s | 166 movl %sp@(4),%a0
187 movl %sp@(4),%a0
199 movl %sp@(4),%a0
213 lea %sp@(4),%a0
251 movl %sp@(4),%a0
261 movl %sp@(4),%a0
272 movl %sp@(4),%a0
289 movl %d2,%sp@- | Toolbox trap may alter %d0-%d2,%a0,%a1
290 | but C caller would save %d1,%a0,%a1
323 movl %sp@(4),%a0
[all...] |
| /src/sys/arch/mips/mips/ |
| spl.S | 67 * a0 = SR bits to be cleared for this IPL
69 * Can only use a0-a3 and v0-v1
81 xor a0, v1 # disable ipl's masked bits
82 DYNAMIC_STATUS_MASK(a0,v0) # machine dependent masking
96 mtc0 a0, MIPS_COP_0_STATUS # store back
106 and a0, v1 # a1 contains bit that MBZ
107 3: bnez a0, 3b # loop forever
116 sltiu v0, a0, IPL_HIGH+1 # v0 = a0 <= IPL_HIGH
124 beq a0, a2, 2f # if same, nothing to d
[all...] |
| /src/sys/compat/linux/arch/m68k/ |
| linux_machdep.c | 141 kf.sf_c.c_sc.sc_a0 = frame->f_regs[A0];
578 frame->f_regs[A0] = scp->sc_a0;
|
| /src/sys/arch/arc/arc/ |
| minidebug.c | 110 "zero", "at", "v0", "v1", "a0", "a1", "a2", "a3",
228 printf("T8-9 %08x %08x A0-4 %08x %08x %08x %08x\n",
230 mdbpcb.pcb_regs[A0],mdbpcb.pcb_regs[A1],
|
| /src/sys/arch/vax/vax/ |
| intvec.S | 125 INTVEC(softclock, KSTACK); # Software clock interrupt, A0 (IPL 08)
|
| /src/sys/arch/virt68k/virt68k/ |
| locore.s | 122 ASRELOC(tmpstk, %a0)
123 movl %a0,%sp | give ourselves a temporary stack
125 RELOC(edata,%a0) | clear out BSS
129 1: clrl %a0@+
142 RELOC(bootinfo_startup1,%a0)
143 jbsr %a0@ | bootinfo_startup1(endpa, reloff)
152 RELOC(pmap_bootstrap1,%a0)
153 jbsr %a0@ | pmap_bootstrap1(nextpa, reloff)
178 /* phase 2 of pmap setup, returns pointer to lwp0 uarea in %a0 */
181 lea %a0@(USPACE-4),%sp | set kernel stack to end of are
[all...] |
| /src/sys/arch/next68k/next68k/ |
| locore.s | 167 RELOC(lowram,%a0) | store base of memory.
168 movl %a5,%a0@
172 ASRELOC(tmpstk, %a0)
173 movel %sp,%a0@-
174 moveal %a0,%sp
178 RELOC(next68k_bootargs,%a0)
179 jbsr %a0@ | next68k_bootargs(args)
199 RELOC(mmutype, %a0) | no, we have 68030
200 movl #MMU_68030,%a0@ | set to reflect 68030 PMMU
201 RELOC(cputype, %a0)
[all...] |
| /src/sys/arch/cesfic/cesfic/ |
| locore.s | 143 movl #0x20000000, %a0
146 movl %a5@+, %a0@+
152 ASRELOC(tmpstk, %a0)
153 movl %a0, %sp | give ourselves a temporary stack
155 RELOC(edata, %a0)
158 clrb %a0@+
159 cmpl %a0, %a1
162 RELOC(esym, %a0)
164 movl %a4, %a0@ | store end of symbol table
166 clrl %a0@ | no symbol table, ye
[all...] |
| /src/sys/arch/luna68k/luna68k/ |
| locore.s | 103 ASRELOC(tmpstk,%a0)
104 movl %a0,%sp | give ourselves a temporary stack
106 RELOC(edata,%a0) | clear out BSS
110 1: clrl %a0@+
113 RELOC(boothowto,%a0)
114 movl %d7,%a0@ | save boothowto
115 RELOC(bootdev,%a0)
116 movl %d6,%a0@ | save bootdev
117 RELOC(lowram,%a0)
118 movl %a5,%a0@ | store start of physical memor
[all...] |
| /src/sys/arch/mvme68k/mvme68k/ |
| locore.s | 115 RELOC(bootpart,%a0)
116 movl %d3, %a0@ | save bootpart
117 RELOC(bootdevlun,%a0)
118 movl %d4, %a0@ | save bootdevlun
119 RELOC(bootctrllun,%a0)
120 movl %d5, %a0@ | save booctrllun
121 RELOC(bootaddr,%a0)
122 movl %d6, %a0@ | save bootaddr
123 RELOC(boothowto,%a0)
124 movl %d7, %a0@ | save boothowt
[all...] |
| /src/sys/arch/news68k/news68k/ |
| locore.s | 97 moveal _ASM_LABEL(monitor), %a0; \
98 jmp %a0@
125 RELOC(bootdev,%a0)
126 movl %d6, %a0@ | save bootdev
127 RELOC(boothowto,%a0)
128 movl %d7, %a0@ | save boothowto
130 ASRELOC(tmpstk,%a0)
131 movl %a0,%sp | give ourselves a temporary stack
133 movc %vbr,%a0
134 movl %a0@(188),_ASM_LABEL(monitor)| save trap #15 to return PROM monito
[all...] |
| /src/sys/arch/x68k/x68k/ |
| locore.s | 123 RELOC(vectab,%a0) | set Vector Base Register temporarily
124 movc %a0,%vbr
127 RELOC(edata, %a0) | clear out BSS
131 1: clrl %a0@+
135 ASRELOC(tmpstk, %a0)
136 movl %a0,%sp | give ourselves a temporary stack
137 RELOC(esym, %a0)
139 movl %a4,%a0@ | store end of symbol table
141 clrl %a0@ | no symbol table, yet
143 RELOC(boothowto, %a0)
[all...] |
