Home
last modified time | relevance | path

Searched +full:1 +full:w (Results 1 – 25 of 1158) sorted by relevance

12345678910>>...47

/Linux-v6.1/arch/sh/drivers/pci/
Dpcie-sh7786.h13 #define SH4A_PCIE_SPW_BASE1 0xFE200000 /* spw config address for controller 1 (Rev1.14)*/
18 #define SH4A_PCI_CNFG_BASE1 0xFE240000 /* pci config address for controller 1 (Rev1.14)*/
44 #define BITS_BADOPC (5) /* 5 BADOPC 0 R/W */
45 #define MASK_BADOPC (1<<BITS_BADOPC)
46 #define BITS_BADDEST (4) /*4 BADDEST 0 R/W */
47 #define MASK_BADDEST (1<<BITS_BADDEST)
48 #define BITS_UNSOLRESP (3) /* 3 UNSOLRESP 0 R/W */
49 #define MASK_UNSOLRESP (1<<BITS_UNSOLRESP)
50 #define BITS_ERRSNT (1) /* 1 ERRSNT 0 */
51 #define MASK_ERRSNT (1<<BITS_ERRSNT)
[all …]
/Linux-v6.1/include/asm-generic/bitops/
Dconst_hweight.h8 #define __const_hweight8(w) \ argument
10 ((!!((w) & (1ULL << 0))) + \
11 (!!((w) & (1ULL << 1))) + \
12 (!!((w) & (1ULL << 2))) + \
13 (!!((w) & (1ULL << 3))) + \
14 (!!((w) & (1ULL << 4))) + \
15 (!!((w) & (1ULL << 5))) + \
16 (!!((w) & (1ULL << 6))) + \
17 (!!((w) & (1ULL << 7)))))
19 #define __const_hweight16(w) (__const_hweight8(w) + __const_hweight8((w) >> 8 )) argument
[all …]
/Linux-v6.1/tools/include/asm-generic/bitops/
Dconst_hweight.h8 #define __const_hweight8(w) \ argument
10 ((!!((w) & (1ULL << 0))) + \
11 (!!((w) & (1ULL << 1))) + \
12 (!!((w) & (1ULL << 2))) + \
13 (!!((w) & (1ULL << 3))) + \
14 (!!((w) & (1ULL << 4))) + \
15 (!!((w) & (1ULL << 5))) + \
16 (!!((w) & (1ULL << 6))) + \
17 (!!((w) & (1ULL << 7)))))
19 #define __const_hweight16(w) (__const_hweight8(w) + __const_hweight8((w) >> 8 )) argument
[all …]
/Linux-v6.1/drivers/input/joystick/
Dwalkera0701.c62 static inline void walkera0701_parse_frame(struct walkera_dev *w) in walkera0701_parse_frame() argument
70 crc1 += w->buf[i] & 7; in walkera0701_parse_frame()
71 crc2 += (w->buf[i] & 8) >> 3; in walkera0701_parse_frame()
73 if ((w->buf[10] & 7) != (crc1 & 7)) in walkera0701_parse_frame()
75 if (((w->buf[10] & 8) >> 3) != (((crc1 >> 3) + crc2) & 1)) in walkera0701_parse_frame()
78 crc1 += w->buf[i] & 7; in walkera0701_parse_frame()
79 crc2 += (w->buf[i] & 8) >> 3; in walkera0701_parse_frame()
81 if ((w->buf[23] & 7) != (crc1 & 7)) in walkera0701_parse_frame()
83 if (((w->buf[23] & 8) >> 3) != (((crc1 >> 3) + crc2) & 1)) in walkera0701_parse_frame()
85 val1 = ((w->buf[0] & 7) * 256 + w->buf[1] * 16 + w->buf[2]) >> 2; in walkera0701_parse_frame()
[all …]
/Linux-v6.1/drivers/usb/gadget/udc/
Ds3c2410_udc_regs.h73 #define S3C2410_UDC_FUNCADDR_UPDATE (1 << 7)
75 #define S3C2410_UDC_PWR_ISOUP (1 << 7) /* R/W */
76 #define S3C2410_UDC_PWR_RESET (1 << 3) /* R */
77 #define S3C2410_UDC_PWR_RESUME (1 << 2) /* R/W */
78 #define S3C2410_UDC_PWR_SUSPEND (1 << 1) /* R */
79 #define S3C2410_UDC_PWR_ENSUSPEND (1 << 0) /* R/W */
83 #define S3C2410_UDC_INT_EP4 (1 << 4) /* R/W (clear only) */
84 #define S3C2410_UDC_INT_EP3 (1 << 3) /* R/W (clear only) */
85 #define S3C2410_UDC_INT_EP2 (1 << 2) /* R/W (clear only) */
86 #define S3C2410_UDC_INT_EP1 (1 << 1) /* R/W (clear only) */
[all …]
/Linux-v6.1/arch/m68k/math-emu/
Dfp_util.S9 * 1. Redistributions of source code must retain the above copyright
64 jmi 1f
66 jmi 1f
69 1: printf ,"oops:%p,%p,%p\n",3,%a2@(TASK_MM-8),%a2@(TASK_MM-4),%a2@(TASK_MM)
102 jpl 1f | positive?
103 moveq #1,%d1
105 1: swap %d1
106 move.w #0x3fff+31,%d1
134 lsr.w #8,%d1
136 cmp.w #0xff,%d1 | NaN / Inf?
[all …]
Dfp_decode.h9 * 1. Redistributions of source code must retain the above copyright
74 jmp ([0f:w,%pc,%d0*4])
86 jmp ([0f:w,%pc,%d0*4])
116 jmp ([0f:w,%pc,%d0*4])
136 ext.w %d0
143 jne 1\@f
144 printf PDECODE,"d%d",1,%d0
147 1\@: printf PDECODE,"a%d",1,%d0
151 debug lea "'l'.w,%a0"
154 debug lea "'w'.w,%a0"
[all …]
/Linux-v6.1/drivers/net/wireless/intersil/hostap/
Dhostap_common.h27 #define HFA384X_RID_CNFWDSADDRESS1 0xFC11 /* AP f/w only */
28 #define HFA384X_RID_CNFWDSADDRESS2 0xFC12 /* AP f/w only */
29 #define HFA384X_RID_CNFWDSADDRESS3 0xFC13 /* AP f/w only */
30 #define HFA384X_RID_CNFWDSADDRESS4 0xFC14 /* AP f/w only */
31 #define HFA384X_RID_CNFWDSADDRESS5 0xFC15 /* AP f/w only */
32 #define HFA384X_RID_CNFWDSADDRESS6 0xFC16 /* AP f/w only */
33 #define HFA384X_RID_CNFMULTICASTPMBUFFERING 0xFC17 /* AP f/w only */
44 #define HFA384X_RID_CNFMAXASSOCSTA 0xFC2B /* AP f/w only */
47 #define HFA384X_RID_CNFHOSTAUTHENTICATION 0xFC2E /* AP f/w only */
52 #define HFA384X_RID_CNFAPPCFINFO 0xFC34 /* AP f/w only */
[all …]
/Linux-v6.1/tools/lib/
Dhweight.c12 unsigned int __sw_hweight32(unsigned int w) in __sw_hweight32() argument
15 w -= (w >> 1) & 0x55555555; in __sw_hweight32()
16 w = (w & 0x33333333) + ((w >> 2) & 0x33333333); in __sw_hweight32()
17 w = (w + (w >> 4)) & 0x0f0f0f0f; in __sw_hweight32()
18 return (w * 0x01010101) >> 24; in __sw_hweight32()
20 unsigned int res = w - ((w >> 1) & 0x55555555); in __sw_hweight32()
28 unsigned int __sw_hweight16(unsigned int w) in __sw_hweight16() argument
30 unsigned int res = w - ((w >> 1) & 0x5555); in __sw_hweight16()
36 unsigned int __sw_hweight8(unsigned int w) in __sw_hweight8() argument
38 unsigned int res = w - ((w >> 1) & 0x55); in __sw_hweight8()
[all …]
/Linux-v6.1/lib/
Dhweight.c13 unsigned int __sw_hweight32(unsigned int w) in __sw_hweight32() argument
16 w -= (w >> 1) & 0x55555555; in __sw_hweight32()
17 w = (w & 0x33333333) + ((w >> 2) & 0x33333333); in __sw_hweight32()
18 w = (w + (w >> 4)) & 0x0f0f0f0f; in __sw_hweight32()
19 return (w * 0x01010101) >> 24; in __sw_hweight32()
21 unsigned int res = w - ((w >> 1) & 0x55555555); in __sw_hweight32()
30 unsigned int __sw_hweight16(unsigned int w) in __sw_hweight16() argument
32 unsigned int res = w - ((w >> 1) & 0x5555); in __sw_hweight16()
39 unsigned int __sw_hweight8(unsigned int w) in __sw_hweight8() argument
41 unsigned int res = w - ((w >> 1) & 0x55); in __sw_hweight8()
[all …]
/Linux-v6.1/arch/x86/crypto/
Dsha1_ssse3_asm.S3 * This is a SIMD SHA-1 implementation. It requires the Intel(R) Supplemental
17 … http://software.intel.com/en-us/articles/improving-the-performance-of-the-secure-hash-algorithm-1/
61 /* we keep window of 64 w[i]+K pre-calculated values in a circular buffer */
66 * This macro implements the SHA-1 function's body for single 64-byte block
108 * This macro implements 80 rounds of SHA-1 for one 64-byte block
122 .set i, (i+1)
126 1:
187 jne 1b
249 * RR does two rounds of SHA-1 back to back with W[] pre-calc
250 * t1 = F(b, c, d); e += w(i)
[all …]
Dsha512-ssse3-asm.S84 # WK_2(t) points to 1 of 2 qwords at frame.WK depdending on t being odd/even
98 # W[t]+K[t] (stack frame)
125 add WK_2(idx), T1 # W[t] + K[t] from message scheduler
129 add h_64, T1 # T1 = CH(e,f,g) + W[t] + K[t] + h
131 add tmp0, T1 # T1 = CH(e,f,g) + W[t] + K[t] + S1(e)
151 # Compute rounds t-2 and t-1
152 # Compute message schedule QWORDS t and t+1
154 # Two rounds are computed based on the values for K[t-2]+W[t-2] and
155 # K[t-1]+W[t-1] which were previously stored at WK_2 by the message
157 # The two new schedule QWORDS are stored at [W_t(%%t)] and [W_t(%%t+1)].
[all …]
Dsha512-avx-asm.S77 # W[t] + K[t] | W[t+1] + K[t+1]
86 # WK_2(t) points to 1 of 2 qwords at frame.WK depdending on t being odd/even
100 # W[t]+K[t] (stack frame)
131 add WK_2(idx), T1 # W[t] + K[t] from message scheduler
135 add h_64, T1 # T1 = CH(e,f,g) + W[t] + K[t] + h
137 add tmp0, T1 # T1 = CH(e,f,g) + W[t] + K[t] + S1(e)
156 # Compute rounds t-2 and t-1
157 # Compute message schedule QWORDS t and t+1
159 # Two rounds are computed based on the values for K[t-2]+W[t-2] and
160 # K[t-1]+W[t-1] which were previously stored at WK_2 by the message
[all …]
/Linux-v6.1/drivers/scsi/
Dnsp32.h33 MODEL_KME = 1,
65 # define TRUE 1
70 #define ASSERT 1
81 #define IRQ_CONTROL 0x00 /* BASE+00, W, W */
82 #define IRQ_STATUS 0x00 /* BASE+00, W, R */
84 # define IRQSTATUS_LATCHED_IO BIT(1)
112 #define TRANSFER_CONTROL 0x02 /* BASE+02, W, W */
113 #define TRANSFER_STATUS 0x02 /* BASE+02, W, R */
115 # define CB_IO_MODE BIT(1)
130 #define INDEX_REG 0x04 /* BASE+04, Byte(R/W), Word(R) */
[all …]
/Linux-v6.1/drivers/video/fbdev/omap/
Dlcd_dma.c42 return 1; in omap_lcd_dma_running()
47 return 1; in omap_lcd_dma_running()
137 u16 w; in set_b1_regs() local
145 es = 1; in set_b1_regs()
159 xscale = lcd_dma.xscale ? lcd_dma.xscale : 1; in set_b1_regs()
160 yscale = lcd_dma.yscale ? lcd_dma.yscale : 1; in set_b1_regs()
165 #define PIXSTEP(sx, sy, dx, dy) (PIXADDR(dx, dy) - PIXADDR(sx, sy) - es + 1) in set_b1_regs()
171 bottom = PIXADDR(lcd_dma.xres - 1, lcd_dma.yres - 1); in set_b1_regs()
177 ei = PIXSTEP(0, 0, 1, 0); in set_b1_regs()
178 fi = PIXSTEP(lcd_dma.xres - 1, 0, 0, 1); in set_b1_regs()
[all …]
/Linux-v6.1/tools/bpf/bpftool/bash-completion/
Dbpftool12 local w idx found
13 for w in $*; do
15 for (( idx=3; idx < ${#words[@]}-1; idx++ )); do
16 if [[ $w == ${words[idx]} ]]; then
17 found=1
22 COMPREPLY+=( $( compgen -W "$w" -- "$cur" ) )
27 # command line, return 0. Otherwise, return 1.
30 local w idx
31 for w in $*; do
32 for (( idx=3; idx < ${#words[@]}-1; idx++ )); do
[all …]
/Linux-v6.1/lib/mpi/
Dmpi-add.c18 * result in W. U and V may be the same.
20 void mpi_add_ui(MPI w, MPI u, unsigned long v) in mpi_add_ui() argument
30 /* If not space for W (and possible carry), increase space. */ in mpi_add_ui()
31 wsize = usize + 1; in mpi_add_ui()
32 if (w->alloced < wsize) in mpi_add_ui()
33 mpi_resize(w, wsize); in mpi_add_ui()
35 /* These must be after realloc (U may be the same as W). */ in mpi_add_ui()
37 wp = w->d; in mpi_add_ui()
41 wsize = v ? 1:0; in mpi_add_ui()
51 if (usize == 1 && up[0] < v) { in mpi_add_ui()
[all …]
/Linux-v6.1/sound/soc/
Dsoc-dapm.c69 [snd_soc_dapm_pre] = 1,
110 [snd_soc_dapm_pre] = 1,
183 static bool dapm_dirty_widget(struct snd_soc_dapm_widget *w) in dapm_dirty_widget() argument
185 return !list_empty(&w->dirty); in dapm_dirty_widget()
188 static void dapm_mark_dirty(struct snd_soc_dapm_widget *w, const char *reason) in dapm_mark_dirty() argument
190 dapm_assert_locked(w->dapm); in dapm_mark_dirty()
192 if (!dapm_dirty_widget(w)) { in dapm_mark_dirty()
193 dev_vdbg(w->dapm->dev, "Marking %s dirty due to %s\n", in dapm_mark_dirty()
194 w->name, reason); in dapm_mark_dirty()
195 list_add_tail(&w->dirty, &w->dapm->card->dapm_dirty); in dapm_mark_dirty()
[all …]
/Linux-v6.1/net/ipv4/
Dtcp_westwood.c63 struct westwood *w = inet_csk_ca(sk); in tcp_westwood_init() local
65 w->bk = 0; in tcp_westwood_init()
66 w->bw_ns_est = 0; in tcp_westwood_init()
67 w->bw_est = 0; in tcp_westwood_init()
68 w->accounted = 0; in tcp_westwood_init()
69 w->cumul_ack = 0; in tcp_westwood_init()
70 w->reset_rtt_min = 1; in tcp_westwood_init()
71 w->rtt_min = w->rtt = TCP_WESTWOOD_INIT_RTT; in tcp_westwood_init()
72 w->rtt_win_sx = tcp_jiffies32; in tcp_westwood_init()
73 w->snd_una = tcp_sk(sk)->snd_una; in tcp_westwood_init()
[all …]
/Linux-v6.1/drivers/media/platform/ti/omap/
Domap_voutlib.c50 crop->width &= ~1; in omap_vout_default_crop()
51 crop->height &= ~1; in omap_vout_default_crop()
52 crop->left = ((pix->width - crop->width) >> 1) & ~1; in omap_vout_default_crop()
53 crop->top = ((pix->height - crop->height) >> 1) & ~1; in omap_vout_default_crop()
69 try_win = new_win->w; in omap_vout_try_window()
90 try_win.width &= ~1; in omap_vout_try_window()
91 try_win.height &= ~1; in omap_vout_try_window()
97 new_win->w = try_win; in omap_vout_try_window()
126 win->w = new_win->w; in omap_vout_new_window()
132 /* For 24xx limit is 8x to 1/2x scaling. */ in omap_vout_new_window()
[all …]
/Linux-v6.1/arch/powerpc/crypto/
Dsha1-powerpc-asm.S3 * SHA-1 implementation for PowerPC.
23 * iteration; T on iteration t is A on iteration t+1, and so on.
30 #define RD(t) ((((t)+1)%6)+7)
33 /* We use registers 16 - 31 for the W values */
34 #define W(t) (((t)%16)+16) macro
37 LWZ(W(t),(t)*4,r4)
46 add r14,r0,W(t); \
47 LWZ(W((t)+4),((t)+4)*4,r4); \
58 xor r5,W((t)+4-3),W((t)+4-8); \
60 xor W((t)+4),W((t)+4-16),W((t)+4-14); \
[all …]
Dsha1-spe-asm.S3 * Fast SHA-1 implementation for SPE instruction set (PPC)
107 LOAD_DATA(w0, off) /* 1: W */ \
108 and rT2,b,c; /* 1: F' = B and C */ \
109 LOAD_K##k##1 \
110 andc rT1,d,b; /* 1: F" = ~B and D */ \
111 rotrwi rT0,a,27; /* 1: A' = A rotl 5 */ \
112 or rT2,rT2,rT1; /* 1: F = F' or F" */ \
113 add e,e,rT0; /* 1: E = E + A' */ \
114 rotrwi b,b,2; /* 1: B = B rotl 30 */ \
115 add e,e,w0; /* 1: E = E + W */ \
[all …]
/Linux-v6.1/drivers/media/platform/samsung/s5p-g2d/
Dg2d-hw.c14 #define w(x, a) writel((x), d->regs + (a)) macro
20 w(1, SOFT_RESET_REG); in g2d_reset()
27 w(0, SRC_SELECT_REG); in g2d_set_src_size()
28 w(f->stride & 0xFFFF, SRC_STRIDE_REG); in g2d_set_src_size()
33 w(n, SRC_LEFT_TOP_REG); in g2d_set_src_size()
38 w(n, SRC_RIGHT_BOTTOM_REG); in g2d_set_src_size()
40 w(f->fmt->hw, SRC_COLOR_MODE_REG); in g2d_set_src_size()
45 w(a, SRC_BASE_ADDR_REG); in g2d_set_src_addr()
52 w(0, DST_SELECT_REG); in g2d_set_dst_size()
53 w(f->stride & 0xFFFF, DST_STRIDE_REG); in g2d_set_dst_size()
[all …]
/Linux-v6.1/crypto/
Daegis128-neon-inner.c44 vst1q_u8(state + 16, st.v[1]); in aegis128_save_state_neon()
51 uint8x16_t aegis_aes_round(uint8x16_t w) in aegis_aes_round() argument
56 if (!__builtin_expect(aegis128_have_aes_insn, 1)) { in aegis_aes_round()
68 w = vqtbl1q_u8(w, vld1q_u8(shift_rows)); in aegis_aes_round()
72 v = vqtbl4q_u8(vld1q_u8_x4(crypto_aes_sbox), w); in aegis_aes_round()
73 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x40), w - 0x40); in aegis_aes_round()
74 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x80), w - 0x80); in aegis_aes_round()
75 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0xc0), w - 0xc0); in aegis_aes_round()
77 asm("tbl %0.16b, {v16.16b-v19.16b}, %1.16b" : "=w"(v) : "w"(w)); in aegis_aes_round()
78 w -= 0x40; in aegis_aes_round()
[all …]
/Linux-v6.1/fs/xfs/libxfs/
Dxfs_trans_space.h29 (((b + XFS_MAX_CONTIG_RMAPS_PER_BLOCK(mp) - 1) / \
35 #define XFS_EXTENTADD_SPACE_RES(mp,w) (XFS_BM_MAXLEVELS(mp,w) - 1) argument
36 #define XFS_NEXTENTADD_SPACE_RES(mp,b,w)\ argument
37 (((b + XFS_MAX_CONTIG_EXTENTS_PER_BLOCK(mp) - 1) / \
39 XFS_EXTENTADD_SPACE_RES(mp,w))
42 #define XFS_SWAP_RMAP_SPACE_RES(mp,b,w)\ argument
43 (XFS_NEXTENTADD_SPACE_RES((mp), (b), (w)) + \
46 #define XFS_DAENTER_1B(mp,w) \ argument
47 ((w) == XFS_DATA_FORK ? (mp)->m_dir_geo->fsbcount : 1)
48 #define XFS_DAENTER_DBS(mp,w) \ argument
[all …]

12345678910>>...47