| /freebsd/sys/arm/include/ |
| H A D | sysreg.h | 43 #define CP14_DBGDIDR(rr) p14, 0, rr, c0, c0, 0 /* Debug ID Register */ 44 #define CP14_DBGDSCRext_V6(rr) p14, 0, rr, c0, c1, 0 /* Debug Status and Ctrl Register v6 */ 45 #define CP14_DBGDSCRext_V7(rr) p14, 0, rr, c0, c2, 2 /* Debug Status and Ctrl Register v7 */ 46 #define CP14_DBGVCR(rr) p14, 0, rr, c0, c7, 0 /* Vector Catch Register */ 47 #define CP14_DBGOSLAR(rr) p14, 0, rr, c1, c0, 4 /* OS Lock Access Register */ 48 #define CP14_DBGOSLSR(rr) p14, 0, rr, c1, c1, 4 /* OS Lock Status Register */ 49 #define CP14_DBGOSDLR(rr) p14, 0, rr, c1, c3, 4 /* OS Double Lock Register */ 50 #define CP14_DBGPRSR(rr) p14, 0, rr, c1, c5, 4 /* Device Powerdown and Reset Status */ 55 * CP15 C0 registers 57 #define CP15_MIDR(rr) p15, 0, rr, c0, c0, 0 /* Main ID Register */ [all …]
|
| /freebsd/crypto/openssl/crypto/bn/ |
| H A D | bn_asm.c | 32 ap += 4; in bn_mul_add_words() 33 rp += 4; in bn_mul_add_words() 34 num -= 4; in bn_mul_add_words() 61 ap += 4; in bn_mul_words() 62 rp += 4; in bn_mul_words() 63 num -= 4; in bn_mul_words() 85 sqr(r[4], r[5], a[2]); in bn_sqr_words() 87 a += 4; in bn_sqr_words() 89 n -= 4; in bn_sqr_words() 122 ap += 4; in bn_mul_add_words() [all …]
|
| /freebsd/crypto/openssl/crypto/bn/asm/ |
| H A D | co-586.pl | 18 &bn_mul_comba("bn_mul_comba4",4); 20 &bn_sqr_comba("bn_sqr_comba4",4); 28 local($a,$ai,$b,$bi,$c0,$c1,$c2,$pos,$i,$na,$nb)=@_; 36 # &mov("eax",&DWP($ai*4,$a,"",0)) ; 37 # &mov("edx",&DWP($bi*4,$b,"",0)); 40 &add($c0,"eax"); 41 &mov("eax",&DWP(($na)*4,$a,"",0)) if $pos == 0; # load next a 45 &mov("edx",&DWP(($nb)*4,$b,"",0)) if $pos == 0; # load next b 46 &mov("edx",&DWP(($nb)*4,$b,"",0)) if $pos == 1; # load next b 50 &mov(&DWP($i*4,"eax","",0),$c0) if $pos > 0; # save r[]; [all …]
|
| H A D | x86_64-gcc.c | 123 ap += 4; in bn_mul_add_words() 124 rp += 4; in bn_mul_add_words() 125 num -= 4; in bn_mul_add_words() 153 ap += 4; in bn_mul_words() 154 rp += 4; in bn_mul_words() 155 num -= 4; in bn_mul_words() 177 sqr(r[4], r[5], a[2]); in bn_sqr_words() 179 a += 4; in bn_sqr_words() 181 n -= 4; in bn_sqr_words() 190 sqr(r[4], r[5], a[2]); in bn_sqr_words() [all …]
|
| /freebsd/sys/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/ |
| H A D | blamka-round-avx512f.h | 17 #define G1_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \ argument 28 C0 = muladd(C0, D0); \ 31 B0 = _mm512_xor_si512(B0, C0); \ 38 #define G2_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \ argument 49 C0 = muladd(C0, D0); \ 52 B0 = _mm512_xor_si512(B0, C0); \ 59 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument 64 C0 = _mm512_permutex_epi64(C0, _MM_SHUFFLE(1, 0, 3, 2)); \ 71 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument 76 C0 = _mm512_permutex_epi64(C0, _MM_SHUFFLE(1, 0, 3, 2)); \ [all …]
|
| H A D | blamka-round-avx2.h | 8 …24(x) _mm256_shuffle_epi8(x, _mm256_setr_epi8(3, 4, 5, 6, 7, 0, 1, 2, 11, 12, 13, 14, 15, 8, 9, 10… 9 …x) _mm256_shuffle_epi8(x, _mm256_setr_epi8(2, 3, 4, 5, 6, 7, 0, 1, 10, 11, 12, 13, 14, 15, 8, 9, 2… 12 #define G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument 20 ml = _mm256_mul_epu32(C0, D0); \ 22 C0 = _mm256_add_epi64(C0, _mm256_add_epi64(D0, ml)); \ 24 B0 = _mm256_xor_si256(B0, C0); \ 41 #define G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument 49 ml = _mm256_mul_epu32(C0, D0); \ 51 C0 = _mm256_add_epi64(C0, _mm256_add_epi64(D0, ml)); \ 52 B0 = _mm256_xor_si256(B0, C0); \ [all …]
|
| H A D | blamka-round-ssse3.h | 8 (_mm_setr_epi8(2, 3, 4, 5, 6, 7, 0, 1, 10, 11, 12, 13, 14, 15, 8, 9)) 10 (_mm_setr_epi8(3, 4, 5, 6, 7, 0, 1, 2, 11, 12, 13, 14, 15, 8, 9, 10)) 31 #define G1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument 42 C0 = fBlaMka(C0, D0); \ 45 B0 = _mm_xor_si128(B0, C0); \ 52 #define G2(A0, B0, C0, D0, A1, B1, C1, D1) \ argument 63 C0 = fBlaMka(C0, D0); \ 66 B0 = _mm_xor_si128(B0, C0); \ 73 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument 80 t0 = C0; \ [all …]
|
| /freebsd/contrib/netbsd-tests/ipf/input/ |
| H A D | f24 | 3 c0a8 01fe eb22 0035 002b d9e6 4a82 0100 9 c0a8 0101 0035 eb22 00a9 d7b9 4a82 8180 11 616e 7503 6564 7502 6175 0000 0100 01c0 16 c0a8 0101 cbe7 50c0 1300 0200 0100 0078 17 8c00 0603 6e73 31c0 13c0 1300 0200 0100 19 65c0 17c0 1300 0200 0100 0078 23 c0a8 0101 8c00 0603 756e 61c0 13c0 6b00 25 0100 0100 0018 4700 0481 7f28 03c0 3f00
|
| /freebsd/crypto/openssl/crypto/modes/asm/ |
| H A D | ghash-sparcv9.pl | 19 # The module implements "4-bit" GCM GHASH function and underlying 20 # single multiplication operation in GF(2^128). "4-bit" means that it 121 sll $nlo,4,$nlo 132 srlx $Zlo,4,$Zlo 136 srlx $Zhi,4,$Zhi 144 sll $nlo,4,$nlo 151 srlx $Zlo,4,$Zlo 157 srlx $Zhi,4,$Zhi 167 srlx $Zlo,4,$Zlo 171 srlx $Zhi,4,$Zhi [all …]
|
| /freebsd/contrib/file/tests/ |
| H A D | utf16xmlsvg.testfile | 9 …<path class="st0" d="M2372.4,727.1l-15.1-26.6h-12.6v26.6h-5.6V666h17c11,0,19.2,5.5,19.2,16.6c0,10.… 10 …H2372.4 M2355.1,670.9h-10.5v24.8h10.7c8.3,0,14.1-4.3,14.1-13.1C2369.5,674.8,2362.9,670.9,2355.1,67… 11 …<path class="st0" d="M2308.6,697.7c0,25,20.5,45.4,45.5,45.4c24.8,0,45.3-20.4,45.3-45.4c0-25-20.5-4… 12 …C2329.1,652.4,2308.6,672.7,2308.6,697.7 M2312.6,697.7c0-22.9,18.5-41.5,41.6-41.5c22.6,0,41.3,18.6,… 13 c0,22.9-18.7,41.5-41.3,41.5C2331.1,739.2,2312.6,720.6,2312.6,697.7"/> 14 …<path class="st0" d="M255.7,469.2c0-188.4,153.3-342.1,342.4-342.1c102.7,0,195.2,46.5,258,118l-219.… 17 …c-23.8,0-45.5,12.3-58.4,24.9c-13.4,12.9-155.3,154.4-168.9,168.6c0,0-24.3,31-72.3,31l-159.9,0c2.2,2… 19 …-66.1l-136.3,0c-23.9,0-46.7,12.7-59.9,24.9c-15.3,14.1-154.3,154-168.4,167.9c0,0-23.3,31.1-71.3,31.1 21 …342.1l-83.7-0.1c-23.9,0-47.5,11.9-59.9,24.9C784,506.8,642.9,652,629.5,665.1c0,0-25.3,31.1-73.3,31.1 23 …c0-40.1,39.9-61.3,82-61.3c40.6,0,94.2,17.3,102.7,80.2h96.1V509.7z M1912.2,218.8h-162.1l-91.3,352.1… [all …]
|
| /freebsd/crypto/openssl/crypto/whrlpool/ |
| H A D | wp_block.c | 159 * 4KB large unconditionally. Otherwise if ROTATE is defined, the 163 * could handle unaligned load as 4KB table doesn't trash the cache, 181 # define LL(c0,c1,c2,c3,c4,c5,c6,c7) c0,c1,c2,c3,c4,c5,c6,c7 argument 182 # define C0(K,i) (Cx.q[K.c[(i)*8+0]]) macro 186 # define C4(K,i) ROTATE(Cx.q[K.c[(i)*8+4]],32) 192 # define LL(c0,c1,c2,c3,c4,c5,c6,c7) c0,c1,c2,c3,c4,c5,c6,c7, \ argument 193 c7,c0,c1,c2,c3,c4,c5,c6, \ 194 c6,c7,c0,c1,c2,c3,c4,c5, \ 195 c5,c6,c7,c0,c1,c2,c3,c4, \ 196 c4,c5,c6,c7,c0,c1,c2,c3, \ [all …]
|
| /freebsd/secure/caroot/trusted/ |
| H A D | Actalis_Authentication_Root_CA.pem | 33 4d:00:96:5a:6f:2f:c0:44:7e:a3:0e:e4:91:cd:58: 35 1d:f5:41:2d:2f:4c:fd:28:ad:e0:8a:ad:22:b4:56: 37 ba:cd:f0:7d:13:57:c0:5d:d2:83:6b:48:4c:c4:ab: 43 47:1f:04:eb:a3:39:92:06:9f:99:d3:bf:d3:ea:4f: 45 10:e7:54:3e:a8:3a:76:24:4f:81:21:c5:e3:0f:02: 48 bc:3e:ed:85:6d:ef:25:11:f2:97:1a:42:61:f7:4a: 50 ff:18:fb:c6:f1:5a:8b:59:e2:02:ac:7b:92:d0:4e: 51 14:4f:59:45:f6:0c:5e:28:5f:b0:e8:3f:45:cf:cf: 53 bc:c0:4a:8f:4a:93:f8:44:21:e2:31:45:61:50:4e: 54 10:d8:e3:35:7c:4c:19:b4:de:05:bf:a3:06:9f:c8: [all …]
|
| /freebsd/contrib/bearssl/src/kdf/ |
| H A D | shake.c | 69 uint64_t c0, c1, c2, c3, c4, bnn; in process_block() local 82 tt2 = A[ 4] ^ A[ 9]; in process_block() 108 tt0 = A[ 4] ^ A[ 9]; in process_block() 148 A[ 4] = A[ 4] ^ t4; in process_block() 172 A[ 4] = (A[ 4] << 27) | (A[ 4] >> (64 - 27)); in process_block() 179 c0 = A[ 0] ^ kt; in process_block() 188 A[ 0] = c0; in process_block() 195 c0 = A[ 3] ^ kt; in process_block() 204 A[ 3] = c0; in process_block() 211 c0 = A[ 1] ^ kt; in process_block() [all …]
|
| /freebsd/sys/contrib/zstd/lib/dictBuilder/ |
| H A D | divsufsort.c | 141 -1,0,1,1,2,2,2,2,3,3,3,3,3,3,3,3,4,4,4,4,4,4,4,4,4,4,4,4,4,4,4,4, 217 return sqq_table[x] >> 4; in ss_isqrt() 755 if(((c) & 4) && ((ss_compare(T, PA + GETIDX(*((b) - 1)), PA + *(b), depth) == 0))) {\ in ss_swapmerge() 801 if(first < lm) { for(; *--l < 0;) { } next |= 4; } in ss_swapmerge() 810 STACK_PUSH(r, rm, last, (next & 3) | (check & 4)); in ss_swapmerge() 811 middle = lm, last = l, check = (check & 3) | (next & 4); in ss_swapmerge() 814 STACK_PUSH(first, lm, l, (check & 3) | (next & 4)); in ss_swapmerge() 815 first = r, middle = rm, check = (next & 3) | (check & 4); in ss_swapmerge() 1409 /* trbudget_init(&budget, tr_ilg(n) * 3 / 4, n); */ in trsort() 1450 int c0, c1; in sort_typeBstar() local [all …]
|
| /freebsd/crypto/openssl/test/recipes/15-test_ml_dsa_codecs_data/ |
| H A D | prv-44-priv.txt | 3 d7:b2:b4:72:54:aa:e0:db:45:e7:93:0d:4a:98:d2: 6 fe:47:34:bd:95:f4:35:ff:9a:61:3a:a5:4a:a4:1c: 7 2c:69:4c:04:32:9a:07:b1:fa:bb:48:f5:2a:30:9f: 9 be:e3:36:85:85:4a:88:26:9d:a3:20:d5:12:0b:fc: 10 fe:89:a1:8e:30:f7:11:4d:83:aa:40:4a:64:6b:6c: 13 40:28:98:14:61:48:a6:61:4c:42:48:a1:92:08:c2: 15 14:09:14:83:6c:18:a7:80:84:10:6e:c9:c0:70:22: 17 00:46:22:93:20:41:06:2e:42:b6:4c:01:16:49:14: 18 28:4c:41:a8:51:80:46:0a:51:16:51:5a:08:20:02: 19 22:44:dc:98:49:d1:32:51:e1:30:65:d3:c0:85:92: [all …]
|
| H A D | prv-44-seed.txt | 7 d7:b2:b4:72:54:aa:e0:db:45:e7:93:0d:4a:98:d2: 10 fe:47:34:bd:95:f4:35:ff:9a:61:3a:a5:4a:a4:1c: 11 2c:69:4c:04:32:9a:07:b1:fa:bb:48:f5:2a:30:9f: 13 be:e3:36:85:85:4a:88:26:9d:a3:20:d5:12:0b:fc: 14 fe:89:a1:8e:30:f7:11:4d:83:aa:40:4a:64:6b:6c: 17 40:28:98:14:61:48:a6:61:4c:42:48:a1:92:08:c2: 19 14:09:14:83:6c:18:a7:80:84:10:6e:c9:c0:70:22: 21 00:46:22:93:20:41:06:2e:42:b6:4c:01:16:49:14: 22 28:4c:41:a8:51:80:46:0a:51:16:51:5a:08:20:02: 23 22:44:dc:98:49:d1:32:51:e1:30:65:d3:c0:85:92: [all …]
|
| /freebsd/usr.bin/mkimg/tests/ |
| H A D | img-1x1-4096-gpt.qcow.hex | 15 00002050 00 00 00 00 00 00 b0 00 00 00 00 00 00 00 c0 00 |................| 22 000020c0 00 00 00 00 00 01 90 00 00 00 00 00 00 01 a0 00 |................| 23 000020d0 00 00 00 00 00 01 b0 00 00 00 00 00 00 01 c0 00 |................| 31 00002150 00 00 00 00 00 02 b0 00 00 00 00 00 00 02 c0 00 |................| 38 000021c0 00 00 00 00 00 03 90 00 00 00 00 00 00 03 a0 00 |................| 39 000021d0 00 00 00 00 00 03 b0 00 00 00 00 00 00 03 c0 00 |................| 47 00002250 00 00 00 00 00 04 b0 00 00 00 00 00 00 04 c0 00 |................| 54 000022c0 00 00 00 00 00 05 90 00 00 00 00 00 00 05 a0 00 |................| 55 000022d0 00 00 00 00 00 05 b0 00 00 00 00 00 00 05 c0 00 |................| 63 00002350 00 00 00 00 00 06 b0 00 00 00 00 00 00 06 c0 00 |................| [all …]
|
| H A D | img-63x255-4096-gpt.qcow.hex | 15 00002050 00 00 00 00 00 00 b0 00 00 00 00 00 00 00 c0 00 |................| 22 000020c0 00 00 00 00 00 01 90 00 00 00 00 00 00 01 a0 00 |................| 23 000020d0 00 00 00 00 00 01 b0 00 00 00 00 00 00 01 c0 00 |................| 31 00002150 00 00 00 00 00 02 b0 00 00 00 00 00 00 02 c0 00 |................| 38 000021c0 00 00 00 00 00 03 90 00 00 00 00 00 00 03 a0 00 |................| 39 000021d0 00 00 00 00 00 03 b0 00 00 00 00 00 00 03 c0 00 |................| 47 00002250 00 00 00 00 00 04 b0 00 00 00 00 00 00 04 c0 00 |................| 54 000022c0 00 00 00 00 00 05 90 00 00 00 00 00 00 05 a0 00 |................| 55 000022d0 00 00 00 00 00 05 b0 00 00 00 00 00 00 05 c0 00 |................| 63 00002350 00 00 00 00 00 06 b0 00 00 00 00 00 00 06 c0 00 |................| [all …]
|
| H A D | img-1x1-4096-apm.qcow.hex | 13 00002030 00 00 00 00 00 00 b0 00 00 00 00 00 00 00 c0 00 |................| 21 000020b0 00 00 00 00 00 01 b0 00 00 00 00 00 00 01 c0 00 |................| 22 000020c0 00 00 00 00 00 01 d0 00 00 00 00 00 00 01 e0 00 |................| 29 00002130 00 00 00 00 00 02 b0 00 00 00 00 00 00 02 c0 00 |................| 37 000021b0 00 00 00 00 00 03 b0 00 00 00 00 00 00 03 c0 00 |................| 38 000021c0 00 00 00 00 00 03 d0 00 00 00 00 00 00 03 e0 00 |................| 45 00002230 00 00 00 00 00 04 b0 00 00 00 00 00 00 04 c0 00 |................| 53 000022b0 00 00 00 00 00 05 b0 00 00 00 00 00 00 05 c0 00 |................| 54 000022c0 00 00 00 00 00 05 d0 00 00 00 00 00 00 05 e0 00 |................| 61 00002330 00 00 00 00 00 06 b0 00 00 00 00 00 00 06 c0 00 |................| [all …]
|
| H A D | img-1x1-512-apm.qcow.hex | 13 00002030 00 00 00 00 00 00 b0 00 00 00 00 00 00 00 c0 00 |................| 21 000020b0 00 00 00 00 00 01 b0 00 00 00 00 00 00 01 c0 00 |................| 22 000020c0 00 00 00 00 00 01 d0 00 00 00 00 00 00 01 e0 00 |................| 29 00002130 00 00 00 00 00 02 b0 00 00 00 00 00 00 02 c0 00 |................| 37 000021b0 00 00 00 00 00 03 b0 00 00 00 00 00 00 03 c0 00 |................| 38 000021c0 00 00 00 00 00 03 d0 00 00 00 00 00 00 03 e0 00 |................| 45 00002230 00 00 00 00 00 04 b0 00 00 00 00 00 00 04 c0 00 |................| 53 000022b0 00 00 00 00 00 05 b0 00 00 00 00 00 00 05 c0 00 |................| 54 000022c0 00 00 00 00 00 05 d0 00 00 00 00 00 00 05 e0 00 |................| 61 00002330 00 00 00 00 00 06 b0 00 00 00 00 00 00 06 c0 00 |................| [all …]
|
| H A D | img-63x255-4096-apm.qcow.hex | 13 00002030 00 00 00 00 00 00 b0 00 00 00 00 00 00 00 c0 00 |................| 21 000020b0 00 00 00 00 00 01 b0 00 00 00 00 00 00 01 c0 00 |................| 22 000020c0 00 00 00 00 00 01 d0 00 00 00 00 00 00 01 e0 00 |................| 29 00002130 00 00 00 00 00 02 b0 00 00 00 00 00 00 02 c0 00 |................| 37 000021b0 00 00 00 00 00 03 b0 00 00 00 00 00 00 03 c0 00 |................| 38 000021c0 00 00 00 00 00 03 d0 00 00 00 00 00 00 03 e0 00 |................| 45 00002230 00 00 00 00 00 04 b0 00 00 00 00 00 00 04 c0 00 |................| 53 000022b0 00 00 00 00 00 05 b0 00 00 00 00 00 00 05 c0 00 |................| 54 000022c0 00 00 00 00 00 05 d0 00 00 00 00 00 00 05 e0 00 |................| 61 00002330 00 00 00 00 00 06 b0 00 00 00 00 00 00 06 c0 00 |................| [all …]
|
| /freebsd/crypto/openssl/crypto/chacha/asm/ |
| H A D | chacha-s390x.pl | 26 # Add vx code path: 4x"vertical". 35 # 4x"vertical" submission [on z13] and >3 faster than scalar code. 37 # from chacha-ppc module, which is also 4x"vertical", to handle inputs 53 $SIZE_T=4; 60 my $stdframe=16*$SIZE_T+4*8; 65 my ($a0,$b0,$c0,$d0)=@_; 66 my ($a1,$b1,$c1,$d1)=map(($_&~3)+(($_+1)&3),($a0,$b0,$c0,$d0)); 76 # 0 4 8 12 < even round 83 # 3 4 9 14 121 stm ($xc,$xc_,"$stdframe+4*8+4*$c0($sp)"); # reload pair of 'c's [all …]
|
| /freebsd/sys/contrib/device-tree/Bindings/clock/st/ |
| H A D | st,quadfs.txt | 27 - clock-output-names : From common clock binding. The block has 4 32 4 strings are provided then no clocks will be created 37 clk_s_c0_quadfs: clk-s-c0-quadfs@9103000 { 44 clock-output-names = "clk-s-c0-fs0-ch0", 45 "clk-s-c0-fs0-ch1", 46 "clk-s-c0-fs0-ch2", 47 "clk-s-c0-fs0-ch3";
|
| /freebsd/secure/caroot/untrusted/ |
| H A D | Staat_der_Nederlanden_Root_CA_-_G3.pem | 27 51:e8:85:2a:b3:cc:4a:34:f2:b0:5f:f3:0e:c7:1c: 37 92:db:c0:f6:6c:63:78:cd:ca:4e:3d:b5:e5:52:9b: 40 c1:35:1a:54:75:ef:43:d3:e5:ae:4e:ce:e7:7b:c3: 41 c6:4e:61:51:4b:ab:9a:45:4b:a1:1f:41:bd:48:53: 44 c6:fc:7f:2b:66:1a:ec:8a:e5:d6:cf:4d:f5:63:09: 45 b7:15:39:d6:7b:ac:eb:e3:7c:e9:4e:fc:75:42:c8: 47 5a:37:40:89:d8:85:a4:d7:f1:0b:de:43:19:d4:4a: 52 6c:c9:3b:71:c1:d5:88:b5:65:bc:c0:e8:17:17:07: 57 6a:3c:fd:41:dc:0e:5a:47:b6:ef:97:61:75:4f:d9: 73 f1:92:f3:61:da:90:25:16:65:c0:9f:54:5d:0e:03:3b:5b:77: [all …]
|
| /freebsd/sys/arm/arm/ |
| H A D | cpufunc.c | 4 * SPDX-License-Identifier: BSD-4-Clause 22 * 4. The name of Causality Limited may not be used to endorse or promote 143 __asm __volatile("mrc p15, 1, %0, c0, c0, 1" in get_cachetype_cp15() 150 __asm __volatile("mcr p15, 2, %0, c0, c0, 0" in get_cachetype_cp15() 152 __asm __volatile("mrc p15, 1, %0, c0, c0, 0" in get_cachetype_cp15() 155 (CPUV7_CT_xSIZE_LEN(csize) + 4); in get_cachetype_cp15() 159 __asm __volatile("mcr p15, 2, %0, c0, c0, 0" in get_cachetype_cp15() 161 __asm __volatile("mrc p15, 1, %0, c0, c0, 0" in get_cachetype_cp15()
|