Home
last modified time | relevance | path

Searched refs:msk (Results 1 – 25 of 257) sorted by relevance

1234567891011

/OK3568_Linux_fs/kernel/net/mptcp/
H A Dpm.c15 int mptcp_pm_announce_addr(struct mptcp_sock *msk, in mptcp_pm_announce_addr() argument
19 pr_debug("msk=%p, local_id=%d", msk, addr->id); in mptcp_pm_announce_addr()
21 msk->pm.local = *addr; in mptcp_pm_announce_addr()
22 WRITE_ONCE(msk->pm.add_addr_echo, echo); in mptcp_pm_announce_addr()
23 WRITE_ONCE(msk->pm.add_addr_signal, true); in mptcp_pm_announce_addr()
27 int mptcp_pm_remove_addr(struct mptcp_sock *msk, u8 local_id) in mptcp_pm_remove_addr() argument
29 pr_debug("msk=%p, local_id=%d", msk, local_id); in mptcp_pm_remove_addr()
31 msk->pm.rm_id = local_id; in mptcp_pm_remove_addr()
32 WRITE_ONCE(msk->pm.rm_addr_signal, true); in mptcp_pm_remove_addr()
36 int mptcp_pm_remove_subflow(struct mptcp_sock *msk, u8 local_id) in mptcp_pm_remove_subflow() argument
[all …]
H A Dprotocol.c29 struct mptcp_sock msk; member
48 static struct socket *__mptcp_nmpc_socket(const struct mptcp_sock *msk) in __mptcp_nmpc_socket() argument
50 if (!msk->subflow || READ_ONCE(msk->can_ack)) in __mptcp_nmpc_socket()
53 return msk->subflow; in __mptcp_nmpc_socket()
80 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) in __mptcp_tcp_fallback() argument
82 sock_owned_by_me((const struct sock *)msk); in __mptcp_tcp_fallback()
84 if (likely(!__mptcp_check_fallback(msk))) in __mptcp_tcp_fallback()
87 return msk->first; in __mptcp_tcp_fallback()
90 static int __mptcp_socket_create(struct mptcp_sock *msk) in __mptcp_socket_create() argument
93 struct sock *sk = (struct sock *)msk; in __mptcp_socket_create()
[all …]
H A Dpm_netlink.c133 struct mptcp_sock *msk) in select_local_address() argument
138 spin_lock_bh(&msk->join_list_lock); in select_local_address()
146 if (entry->addr.family == ((struct sock *)msk)->sk_family && in select_local_address()
147 !lookup_subflow_by_saddr(&msk->conn_list, &entry->addr) && in select_local_address()
148 !lookup_subflow_by_saddr(&msk->join_list, &entry->addr)) { in select_local_address()
153 spin_unlock_bh(&msk->join_list_lock); in select_local_address()
182 static void check_work_pending(struct mptcp_sock *msk) in check_work_pending() argument
184 if (msk->pm.add_addr_signaled == msk->pm.add_addr_signal_max && in check_work_pending()
185 (msk->pm.local_addr_used == msk->pm.local_addr_max || in check_work_pending()
186 msk->pm.subflows == msk->pm.subflows_max)) in check_work_pending()
[all …]
H A Dtoken_test.c54 struct mptcp_sock *msk; in build_msk() local
56 msk = kunit_kzalloc(test, sizeof(struct mptcp_sock), GFP_USER); in build_msk()
57 KUNIT_EXPECT_NOT_ERR_OR_NULL(test, msk); in build_msk()
58 refcount_set(&((struct sock *)msk)->sk_refcnt, 1); in build_msk()
59 sock_net_set((struct sock *)msk, &init_net); in build_msk()
60 return msk; in build_msk()
67 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_msk_basic() local
72 ctx->conn = (struct sock *)msk; in mptcp_token_test_msk_basic()
73 sk = (struct sock *)msk; in mptcp_token_test_msk_basic()
78 KUNIT_EXPECT_EQ(test, ctx->token, msk->token); in mptcp_token_test_msk_basic()
[all …]
H A Dprotocol.h245 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_tail() local
247 if (list_empty(&msk->rtx_queue)) in mptcp_rtx_tail()
250 return list_last_entry(&msk->rtx_queue, struct mptcp_data_frag, list); in mptcp_rtx_tail()
255 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_head() local
257 return list_first_entry_or_null(&msk->rtx_queue, struct mptcp_data_frag, list); in mptcp_rtx_head()
274 struct mptcp_sock *msk; member
407 void mptcp_rcv_space_init(struct mptcp_sock *msk, const struct sock *ssk);
412 bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit);
413 void mptcp_destroy_common(struct mptcp_sock *msk);
425 struct mptcp_sock *msk);
[all …]
H A Dmptcp_diag.c32 struct mptcp_sock *msk = NULL; in mptcp_diag_dump_one() local
39 msk = mptcp_token_get_sock(net, req->id.idiag_cookie[0]); in mptcp_diag_dump_one()
40 if (!msk) in mptcp_diag_dump_one()
44 sk = (struct sock *)msk; in mptcp_diag_dump_one()
77 struct mptcp_sock *msk; in mptcp_diag_dump() local
83 while ((msk = mptcp_token_iter_next(net, &cb->args[0], &cb->args[1])) != in mptcp_diag_dump()
85 struct inet_sock *inet = (struct inet_sock *)msk; in mptcp_diag_dump()
86 struct sock *sk = (struct sock *)msk; in mptcp_diag_dump()
116 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_diag_get_info() local
128 info->mptcpi_subflows = READ_ONCE(msk->pm.subflows); in mptcp_diag_get_info()
[all …]
H A Doptions.c489 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_dss() local
497 snd_data_fin_enable = READ_ONCE(msk->snd_data_fin_enable); in mptcp_established_options_dss()
518 if (!READ_ONCE(msk->can_ack)) { in mptcp_established_options_dss()
523 if (READ_ONCE(msk->use_64bit_ack)) { in mptcp_established_options_dss()
525 opts->ext_copy.data_ack = READ_ONCE(msk->ack_seq); in mptcp_established_options_dss()
529 opts->ext_copy.data_ack32 = (uint32_t)READ_ONCE(msk->ack_seq); in mptcp_established_options_dss()
584 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr() local
589 if (!mptcp_pm_should_add_signal(msk) || in mptcp_established_options_add_addr()
590 !(mptcp_pm_add_addr_signal(msk, remaining, &saddr, &echo))) in mptcp_established_options_add_addr()
603 opts->ahmac = add_addr_generate_hmac(msk->local_key, in mptcp_established_options_add_addr()
[all …]
H A Dtoken.c155 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_token_new_connect() local
175 WRITE_ONCE(msk->token, subflow->token); in mptcp_token_new_connect()
176 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain); in mptcp_token_new_connect()
191 struct mptcp_sock *msk) in mptcp_token_accept() argument
203 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain); in mptcp_token_accept()
211 struct mptcp_sock *msk; in mptcp_token_exists() local
219 msk = mptcp_sk(sk); in mptcp_token_exists()
220 if (READ_ONCE(msk->token) == token) in mptcp_token_exists()
247 struct mptcp_sock *msk; in mptcp_token_get_sock() local
255 msk = mptcp_sk(sk); in mptcp_token_get_sock()
[all …]
H A Dsubflow.c39 if (subflow_req->msk) in subflow_req_destructor()
40 sock_put((struct sock *)subflow_req->msk); in subflow_req_destructor()
57 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk) in mptcp_can_accept_new_subflow() argument
59 return mptcp_is_fully_established((void *)msk) && in mptcp_can_accept_new_subflow()
60 READ_ONCE(msk->pm.accept_subflow); in mptcp_can_accept_new_subflow()
69 struct mptcp_sock *msk; in subflow_token_join_request() local
72 msk = mptcp_token_get_sock(sock_net(req_to_sk(req)), subflow_req->token); in subflow_token_join_request()
73 if (!msk) { in subflow_token_join_request()
78 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request()
80 sock_put((struct sock *)msk); in subflow_token_join_request()
[all …]
H A Dsyncookies.c97 struct mptcp_sock *msk; in mptcp_token_join_cookie_init_state() local
111 msk = mptcp_token_get_sock(net, e->token); in mptcp_token_join_cookie_init_state()
112 if (!msk) { in mptcp_token_join_cookie_init_state()
122 subflow_req->msk = msk; in mptcp_token_join_cookie_init_state()
/OK3568_Linux_fs/kernel/arch/powerpc/include/asm/
H A Dfeature-fixups.h39 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
45 FTR_ENTRY_LONG msk; \
61 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
63 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup)
65 #define END_FTR_SECTION(msk, val) \ argument
66 END_FTR_SECTION_NESTED(msk, val, 97)
68 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
69 END_FTR_SECTION_NESTED((msk), (msk), label)
71 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
72 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
[all …]
/OK3568_Linux_fs/kernel/tools/testing/selftests/powerpc/primitives/asm/
H A Dfeature-fixups.h39 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
45 FTR_ENTRY_LONG msk; \
61 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
63 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup)
65 #define END_FTR_SECTION(msk, val) \ argument
66 END_FTR_SECTION_NESTED(msk, val, 97)
68 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
69 END_FTR_SECTION_NESTED((msk), (msk), label)
71 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
72 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
[all …]
/OK3568_Linux_fs/kernel/drivers/net/ethernet/netronome/nfp/flower/
H A Dmatch.c12 struct nfp_flower_meta_tci *msk, in nfp_flower_compile_meta_tci() argument
18 memset(msk, 0, sizeof(struct nfp_flower_meta_tci)); in nfp_flower_compile_meta_tci()
24 msk->nfp_flow_key_layer = key_type; in nfp_flower_compile_meta_tci()
25 msk->mask_id = ~0; in nfp_flower_compile_meta_tci()
44 msk->tci = cpu_to_be16(tmp_tci); in nfp_flower_compile_meta_tci()
79 struct nfp_flower_mac_mpls *msk, struct flow_rule *rule, in nfp_flower_compile_mac() argument
83 memset(msk, 0, sizeof(struct nfp_flower_mac_mpls)); in nfp_flower_compile_mac()
92 ether_addr_copy(msk->mac_dst, &match.mask->dst[0]); in nfp_flower_compile_mac()
93 ether_addr_copy(msk->mac_src, &match.mask->src[0]); in nfp_flower_compile_mac()
124 msk->mpls_lse = cpu_to_be32(t_mpls); in nfp_flower_compile_mac()
[all …]
/OK3568_Linux_fs/external/xserver/mi/
H A Dmipushpxl.c100 MiBits msk; in miPushPixels() local
141 msk = startmask; in miPushPixels()
143 msk = (MiBits) (-1) ^ SCRRIGHT((MiBits) (-1), 1); in miPushPixels()
146 if (w & msk) { in miPushPixels()
171 msk = in miPushPixels()
172 LONG2CHARSSAMEORDER(LONG2CHARSSAMEORDER(msk) << 1); in miPushPixels()
174 msk = in miPushPixels()
175 LONG2CHARSSAMEORDER(LONG2CHARSSAMEORDER(msk) >> 1); in miPushPixels()
177 msk = LONG2CHARSDIFFORDER(LONG2CHARSDIFFORDER(msk) << 1); in miPushPixels()
179 msk = LONG2CHARSDIFFORDER(LONG2CHARSDIFFORDER(msk) >> 1); in miPushPixels()
[all …]
/OK3568_Linux_fs/u-boot/arch/x86/cpu/quark/
H A Dmrc_util.c142 uint32_t msk; in set_rcvn() local
157 msk = (byte_lane & 1) ? 0xf00000 : 0xf00; in set_rcvn()
160 mrc_alt_write_mask(DDRPHY, reg, temp, msk); in set_rcvn()
173 msk = 0x3f000000; in set_rcvn()
175 mrc_alt_write_mask(DDRPHY, reg, temp, msk); in set_rcvn()
184 msk = 0x00; in set_rcvn()
188 msk |= (byte_lane & 1) ? (1 << 5) : (1 << 2); in set_rcvn()
190 temp |= msk; in set_rcvn()
193 msk |= (byte_lane & 1) ? (1 << 11) : (1 << 8); in set_rcvn()
195 temp |= msk; in set_rcvn()
[all …]
/OK3568_Linux_fs/kernel/kernel/irq/
H A Dmatrix.c130 const struct cpumask *msk) in matrix_find_best_cpu() argument
137 for_each_cpu(cpu, msk) { in matrix_find_best_cpu()
151 const struct cpumask *msk) in matrix_find_best_cpu_managed() argument
158 for_each_cpu(cpu, msk) { in matrix_find_best_cpu_managed()
210 int irq_matrix_reserve_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_reserve_managed() argument
214 for_each_cpu(cpu, msk) { in irq_matrix_reserve_managed()
231 for_each_cpu(cpu, msk) { in irq_matrix_reserve_managed()
251 void irq_matrix_remove_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_remove_managed() argument
255 for_each_cpu(cpu, msk) { in irq_matrix_remove_managed()
285 int irq_matrix_alloc_managed(struct irq_matrix *m, const struct cpumask *msk, in irq_matrix_alloc_managed() argument
[all …]
H A Ddevres.c235 u32 msk; member
244 irq_remove_generic_chip(this->gc, this->msk, this->clr, this->set); in devm_irq_remove_generic_chip()
263 u32 msk, enum irq_gc_flags flags, in devm_irq_setup_generic_chip() argument
273 irq_setup_generic_chip(gc, msk, flags, clr, set); in devm_irq_setup_generic_chip()
276 dr->msk = msk; in devm_irq_setup_generic_chip()
/OK3568_Linux_fs/kernel/drivers/clk/sprd/
H A Dpll.c54 u32 msk, u32 val) in sprd_pll_write() argument
66 regmap_write(common->regmap, offset, (reg & ~msk) | val); in sprd_pll_write()
173 cfg[index].msk = mask; in _sprd_pll_set_rate()
184 cfg[index].msk |= mask; in _sprd_pll_set_rate()
189 cfg[index].msk |= mask; in _sprd_pll_set_rate()
196 cfg[index].msk |= mask; in _sprd_pll_set_rate()
206 cfg[index].msk |= mask; in _sprd_pll_set_rate()
214 cfg[index].msk |= mask; in _sprd_pll_set_rate()
217 if (cfg[i].msk) { in _sprd_pll_set_rate()
218 sprd_pll_write(pll, i, cfg[i].msk, cfg[i].val); in _sprd_pll_set_rate()
[all …]
/OK3568_Linux_fs/kernel/drivers/media/usb/pvrusb2/
H A Dpvrusb2-ctrl.c207 int msk; in pvr2_ctrl_get_valname() local
210 for (idx = 0, msk = 1; val; idx++, msk <<= 1) { in pvr2_ctrl_get_valname()
211 if (val & msk) { in pvr2_ctrl_get_valname()
291 static unsigned int gen_bitmask_string(int msk,int val,int msk_only, in gen_bitmask_string() argument
304 for (idx = 0, sm = 1; msk; idx++, sm <<= 1) { in gen_bitmask_string()
305 if (sm & msk) { in gen_bitmask_string()
306 msk &= ~sm; in gen_bitmask_string()
396 int msk; in parse_mtoken() local
398 for (idx = 0, msk = 1; valid_bits; idx++, msk <<= 1) { in parse_mtoken()
399 if (!(msk & valid_bits)) continue; in parse_mtoken()
[all …]
/OK3568_Linux_fs/u-boot/arch/m68k/cpu/mcf5227x/
H A Dcpu.c34 u16 msk; in checkcpu() local
39 msk = (in_be16(&ccm->cir) >> 6); in checkcpu()
41 switch (msk) { in checkcpu()
50 printf("Freescale MCF%d (Mask:%01x Version:%x)\n", id, msk, in checkcpu()
/OK3568_Linux_fs/kernel/drivers/net/ethernet/aquantia/atlantic/
H A Daq_hw_utils.c19 void aq_hw_write_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, in aq_hw_write_reg_bit() argument
22 if (msk ^ ~0) { in aq_hw_write_reg_bit()
26 reg_new = (reg_old & (~msk)) | (val << shift); in aq_hw_write_reg_bit()
35 u32 aq_hw_read_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, u32 shift) in aq_hw_read_reg_bit() argument
37 return ((aq_hw_read_reg(aq_hw, addr) & msk) >> shift); in aq_hw_read_reg_bit()
/OK3568_Linux_fs/u-boot/arch/m68k/cpu/mcf523x/
H A Dcpu.c34 u16 msk; in checkcpu() local
39 msk = (in_be16(&ccm->cir) >> 6); in checkcpu()
41 switch (msk) { in checkcpu()
50 printf("Freescale MCF%d (Mask:%01x Version:%x)\n", id, msk, in checkcpu()
/OK3568_Linux_fs/kernel/lib/vdso/
H A Dgettimeofday.c228 u32 msk; in __cvdso_clock_gettime_common() local
238 msk = 1U << clock; in __cvdso_clock_gettime_common()
239 if (likely(msk & VDSO_HRES)) in __cvdso_clock_gettime_common()
241 else if (msk & VDSO_COARSE) in __cvdso_clock_gettime_common()
243 else if (msk & VDSO_RAW) in __cvdso_clock_gettime_common()
357 u32 msk; in __cvdso_clock_getres_common() local
372 msk = 1U << clock; in __cvdso_clock_getres_common()
373 if (msk & (VDSO_HRES | VDSO_RAW)) { in __cvdso_clock_getres_common()
378 } else if (msk & VDSO_COARSE) { in __cvdso_clock_getres_common()
/OK3568_Linux_fs/u-boot/arch/m68k/cpu/mcf5445x/
H A Dcpu.c37 u16 msk; in checkcpu() local
42 msk = (in_be16(&ccm->cir) >> 6); in checkcpu()
44 switch (msk) { in checkcpu()
83 printf("Freescale MCF%d (Mask:%01x Version:%x)\n", id, msk, in checkcpu()
/OK3568_Linux_fs/u-boot/arch/m68k/cpu/mcf532x/
H A Dcpu.c36 u16 msk; in checkcpu() local
41 msk = (in_be16(&ccm->cir) >> 6); in checkcpu()
43 switch (msk) { in checkcpu()
89 printf("Freescale MCF%d (Mask:%01x Version:%x)\n", id, msk, in checkcpu()

1234567891011