Home
last modified time | relevance | path

Searched refs:b32 (Results 1 – 25 of 76) sorted by relevance

1234

/netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/engine/ce/fuc/
H A Dcom.fuc32 ctx_object: .b32 0
35 ctx_dma_query: .b32 0
36 ctx_dma_src: .b32 0
37 ctx_dma_dst: .b32 0
40 ctx_query_address_high: .b32 0
41 ctx_query_address_low: .b32 0
42 ctx_query_counter: .b32 0
43 ctx_src_address_high: .b32 0
44 ctx_src_address_low: .b32 0
45 ctx_src_pitch: .b32 0
[all …]
/netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/engine/sec/fuc/
H A Dg98.fuc0s23 ctx_dma_query: .b32 0
24 ctx_dma_src: .b32 0
25 ctx_dma_dst: .b32 0
27 ctx_query_address_high: .b32 0
28 ctx_query_address_low: .b32 0
29 ctx_query_counter: .b32 0
30 ctx_cond_address_high: .b32 0
31 ctx_cond_address_low: .b32 0
32 ctx_cond_off: .b32 0
33 ctx_src_address_high: .b32 0
[all …]
/netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/engine/gr/fuc/
H A Dgpc.fuc32 gpc_mmio_list_head: .b32 #mmio_list_base
34 tpc_mmio_list_head: .b32 #mmio_list_base
36 unk_mmio_list_head: .b32 #mmio_list_base
37 unk_mmio_list_tail: .b32 #mmio_list_base
39 gpc_id: .b32 0
41 tpc_count: .b32 0
42 tpc_mask: .b32 0
45 unk_count: .b32 0
46 unk_mask: .b32 0
60 */ mov b32 $r15 reg /*
[all …]
H A Dcom.fuc35 ld b32 $r8 D[$r13 + 0x0] // GET
36 ld b32 $r9 D[$r13 + 0x4] // PUT
38 cmpu b32 $r8 $r9
47 shl b32 $r8 3
48 add b32 $r8 $r13
49 add b32 $r8 8
50 st b32 D[$r8 + 0x0] $r14
51 st b32 D[$r8 + 0x4] $r15
54 add b32 $r9 1
56 st b32 D[$r13 + 0x4] $r9
[all …]
H A Dhub.fuc27 hub_mmio_list_head: .b32 #hub_mmio_list_base
28 hub_mmio_list_tail: .b32 #hub_mmio_list_next
30 gpc_count: .b32 0
31 rop_count: .b32 0
34 ctx_current: .b32 0
38 chan_mmio_count: .b32 0
39 chan_mmio_address: .b32 0
45 .b32 0x0417e91c // 0x17e91c, 2
70 clear b32 $r0
76 shl b32 $r1 8
[all …]
H A Dmacros.fuc199 #define mmctx_data(r,c) .b32 (((c - 1) << 26) | r)
241 */ clear b32 $r0
246 */ mov b32 reg $r15
249 */ mov b32 $r15 reg /*
254 */ clear b32 $r9 /*
259 */ clear b32 $r9 /*
/netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/subdev/pmu/fuc/
H A Di2c_.fuc38 .b32 NV_PPWR_OUTPUT_I2C_0_SCL
39 .b32 NV_PPWR_OUTPUT_I2C_1_SCL
40 .b32 NV_PPWR_OUTPUT_I2C_2_SCL
41 .b32 NV_PPWR_OUTPUT_I2C_3_SCL
42 .b32 NV_PPWR_OUTPUT_I2C_4_SCL
43 .b32 NV_PPWR_OUTPUT_I2C_5_SCL
44 .b32 NV_PPWR_OUTPUT_I2C_6_SCL
45 .b32 NV_PPWR_OUTPUT_I2C_7_SCL
46 .b32 NV_PPWR_OUTPUT_I2C_8_SCL
47 .b32 NV_PPWR_OUTPUT_I2C_9_SCL
[all …]
H A Dkernel.fuc36 time_prev: .b32 0
37 time_next: .b32 0
103 sub b32 $r9 $r8
104 cmp b32 $r9 $r14
125 cmp b32 $r10 $r12
128 sub b32 $r9 $r8
129 cmp b32 $r9 $r11
141 ld b32 $r9 D[$r14 + #proc_time]
142 cmp b32 $r9 0
147 ld b32 $r10 D[$r0 + #time_prev]
[all …]
H A Dmemx.fuc43 */ .b32 func
60 .b32 0
62 .b32 0
118 st b32 D[$r0 + #memx_ts_start] $r6
129 st b32 D[$r0 + #memx_ts_end] $r6
172 ld b32 $r6 D[$r1 + 0x00]
173 cmp b32 $r6 0x0
175 cmp b32 $r6 0x1
197 add b32 $r1 0x4
210 add b32 $r1 0x4
[all …]
H A Darith.fuc58 shr b32 $r1 $r14 16
59 shr b32 $r2 $r13 16
61 clear b32 $r12
62 clear b32 $r11
69 mov b32 $r4 $r3
71 shl b32 $r3 16
72 shr b32 $r4 16 // tmp1 = tmp0_hi
73 add b32 $r12 $r3
74 adc b32 $r11 $r4
78 mov b32 $r4 $r3
[all …]
H A Dhost.fuc69 cmp b32 $r1 $r2
73 shl b32 $r14 $r14 #fifo_qlen
74 add b32 $r14 #fifo_queue
77 ld b32 $r11 D[$r14 + #fifo_data1]
78 ld b32 $r12 D[$r14 + #fifo_data0]
79 ld b32 $r13 D[$r14 + #fifo_message]
80 ld b32 $r14 D[$r14 + #fifo_process]
84 add b32 $r1 0x1
102 cmp b32 $r14 $r1
110 cmp b32 $r1 $r2
[all …]
H A Dmacros.fuc164 */ .b32 id /*
165 */ .b32 init /*
166 */ .b32 recv /*
167 */ .b32 0 /*
168 */ .b32 0 /*
169 */ .b32 0 /*
184 */ shl b32 reg 6 /*
195 */ shl b32 $r0 6 /*
197 */ clear b32 $r0
202 */ clear b32 $r0
[all …]
H A Didle.fuc57 add b32 $r1 1
68 mov b32 $r14 $r1
76 add b32 $r1 #proc_size
77 cmp b32 $r1 $r15
/netbsd-src/regress/lib/libc/divrem/
H A Ddivremtest.c83 int32_t a32, b32, sr32; in main() local
94 b32 = 1 << j; in main()
97 TEST("32 ", a32 + k, b32 + l, sr32); in main()
98 TEST("32 ", a32 + k, -(b32 + l), sr32); in main()
99 TEST("32 ", -(a32 + k), b32 + l, sr32); in main()
100 TEST("32 ", -(a32 + k), -(b32 + l), sr32); in main()
111 for(b32 = -NEARBY; b32 < NEARBY; ++b32) { in main()
112 TEST("32 ", a32, b32, sr32); in main()
113 if (a32 >= 0 && b32 >= 0) in main()
114 TEST("32U", (unsigned)a32, (unsigned)b32, ur32); in main()
[all …]
/netbsd-src/external/bsd/unbound/dist/sldns/
H A Dparseutil.c381 const char* b32 = extended_hex ? "0123456789abcdefghijklmnopqrstuv" in sldns_b32_ntop_base() local
402 dst[0] = b32[(src[0] ) >> 3]; in sldns_b32_ntop_base()
405 dst[1] = b32[(src[0] & 0x07) << 2 | src[1] >> 6]; in sldns_b32_ntop_base()
408 dst[2] = b32[(src[1] & 0x3e) >> 1]; in sldns_b32_ntop_base()
411 dst[3] = b32[(src[1] & 0x01) << 4 | src[2] >> 4]; in sldns_b32_ntop_base()
414 dst[4] = b32[(src[2] & 0x0f) << 1 | src[3] >> 7]; in sldns_b32_ntop_base()
417 dst[5] = b32[(src[3] & 0x7c) >> 2]; in sldns_b32_ntop_base()
420 dst[6] = b32[(src[3] & 0x03) << 3 | src[4] >> 5]; in sldns_b32_ntop_base()
423 dst[7] = b32[(src[4] & 0x1f) ]; in sldns_b32_ntop_base()
432 dst[6] = b32[(src[3] & 0x03) << 3]; in sldns_b32_ntop_base()
[all …]
/netbsd-src/lib/libcrypt/
H A Dcrypt.c234 } b32; member
250 rslt = (cvt.b32.i0 & 0x3f3f3f3fL) << 2; \
257 #define LOAD(d,d0,d1,bl) d0 = (bl).b32.i0, d1 = (bl).b32.i1
259 #define OR(d,d0,d1,bl) d0 |= (bl).b32.i0, d1 |= (bl).b32.i1
260 #define STORE(s,s0,s1,bl) (bl).b32.i0 = s0, (bl).b32.i1 = s1
813 B.b32.i0 = k ^ q0 ^ kp->b32 in des_cipher()
[all...]
/netbsd-src/lib/libc/gen/
H A DLint_bswap32.c8 bswap32(u_int32_t b32) in bswap32() argument
/netbsd-src/external/apache2/llvm/dist/llvm/lib/Target/NVPTX/
H A DNVPTXIntrinsics.td159 # mode # ".b32\t"
205 defm VOTE_BALLOT : VOTE<Int32Regs, "ballot.b32", int_nvvm_vote_ballot>;
222 defm VOTE_SYNC_BALLOT : VOTE_SYNC<Int32Regs, "ballot.b32", int_nvvm_vote_ballot_sync>;
244 defm MATCH_ANY_SYNC_32 : MATCH_ANY_SYNC<Int32Regs, "b32", int_nvvm_match_any_sync_i32,
272 defm MATCH_ALLP_SYNC_32 : MATCH_ALLP_SYNC<Int32Regs, "b32", int_nvvm_match_all_sync_i32p,
289 defm REDUX_SYNC_AND : REDUX_SYNC<"and", "b32", int_nvvm_redux_sync_and>;
290 defm REDUX_SYNC_XOR : REDUX_SYNC<"xor", "b32", int_nvvm_redux_sync_xor>;
291 defm REDUX_SYNC_OR : REDUX_SYNC<"or", "b32", int_nvvm_redux_sync_or>;
579 def INT_NVVM_PRMT : F_MATH_3<"prmt.b32 \t$dst, $src0, $src1, $src2;", Int32Regs,
1054 ".reg .b32 %temp; \n\t",
[all …]
H A DNVPTXInstrInfo.td1084 // .b32, .b64, and .pred (predicate registers -- i.e., i1) versions of OpcStr.
1104 !strconcat(OpcStr, ".b32 \t$dst, $a, $b;"),
1108 !strconcat(OpcStr, ".b32 \t$dst, $a, $b;"),
1131 "not.b32 \t$dst, $src;",
1180 "brev.b32 \t$dst, $a;",
1196 "shf.l.wrap.b32 \t$dst, $src, $src, $amt;",
1202 "shf.l.wrap.b32 \t$dst, $src, $src, $amt;",
1211 "shf.r.wrap.b32 \t$dst, $src, $src, $amt;",
1217 "shf.r.wrap.b32 \t$dst, $src, $src, $amt;",
1226 ".reg .b32 %lhs;\n\t"
[all …]
/netbsd-src/external/bsd/nsd/dist/
H A Dutil.c652 static char b32[]="0123456789abcdefghijklmnopqrstuv"; in b32_ntop() local
662 buf[0]=b32[src[0] >> 3]; in b32_ntop()
668 buf[1]=b32[t]; in b32_ntop()
673 buf[2]=b32[(src[1] >> 1)&0x1f]; in b32_ntop()
679 buf[3]=b32[t]; in b32_ntop()
687 buf[4]=b32[t]; in b32_ntop()
692 buf[5]=b32[(src[3] >> 2)&0x1f]; in b32_ntop()
698 buf[6]=b32[t]; in b32_ntop()
703 buf[7]=b32[src[4]&0x1f]; in b32_ntop()
/netbsd-src/external/gpl3/gcc/dist/libgcc/
H A Ddfp-bit.c98 union { _Decimal32 c; decSingle f; } a32, b32, res32; in d32_binary_op() local
104 b32.c = arg_b; in d32_binary_op()
106 decSingleToWider (&b32.f, &b); in d32_binary_op()
177 union { _Decimal32 c; decSingle f; } a32, b32; in d32_compare_op() local
181 b32.c = arg_b; in d32_compare_op()
183 decSingleToWider (&b32.f, &b); in d32_compare_op()
/netbsd-src/external/gpl3/gcc.old/dist/libgcc/
H A Ddfp-bit.c98 union { _Decimal32 c; decSingle f; } a32, b32, res32; in d32_binary_op() local
104 b32.c = arg_b; in d32_binary_op()
106 decSingleToWider (&b32.f, &b); in d32_binary_op()
177 union { _Decimal32 c; decSingle f; } a32, b32; in d32_compare_op() local
181 b32.c = arg_b; in d32_compare_op()
183 decSingleToWider (&b32.f, &b); in d32_compare_op()
/netbsd-src/sys/compat/netbsd32/
H A Dnetbsd32_drm.c393 drm_buf_desc32_t b32; in compat_drm_markbufs() local
397 if ((error = copyin(&b32, arg, sizeof(b32))) != 0) in compat_drm_markbufs()
400 b64.size = b32.size; in compat_drm_markbufs()
401 b64.low_mark = b32.low_mark; in compat_drm_markbufs()
402 b64.high_mark = b32.high_mark; in compat_drm_markbufs()
/netbsd-src/sys/ufs/lfs/
H A Dlfs_accessors.h1408 bp->b32 = p; in lfs_blocks_fromvoid()
1421 bp->b32 = (int32_t *)firstblock; in lfs_blocks_fromfinfo()
1431 return bp->b32[idx]; in lfs_blocks_get()
1441 bp->b32[idx] = val; in lfs_blocks_set()
1451 bp->b32++; in lfs_blocks_inc()
1461 return bp1->b32 == bp2->b32; in lfs_blocks_eq()
1472 return bp1->b32 - bp2->b32; in lfs_blocks_sub()
/netbsd-src/sys/external/bsd/drm2/dist/drm/
H A Ddrm_ioc32.c358 drm_buf_desc32_t b32; in compat_drm_markbufs() local
362 if (copy_from_user(&b32, argp, sizeof(b32))) in compat_drm_markbufs()
365 buf.size = b32.size; in compat_drm_markbufs()
366 buf.low_mark = b32.low_mark; in compat_drm_markbufs()
367 buf.high_mark = b32.high_mark; in compat_drm_markbufs()

1234