Home
last modified time | relevance | path

Searched refs:local_id (Results 1 - 25 of 62) sorted by relevance

123

/kernel/linux/linux-5.10/drivers/infiniband/core/
H A Dcm_trace.h146 __field(unsigned int, local_id)
154 __entry->local_id = be32_to_cpu(cm_id->local_id);
160 TP_printk("local_id=%u remote_id=%u state=%s lap_state=%s",
161 __entry->local_id, __entry->remote_id,
196 __field(u32, local_id)
204 __entry->local_id = be32_to_cpu(cm_id->local_id);
210 TP_printk("local_id=%u remote_id=%u state=%s reason=%s",
211 __entry->local_id, __entr
[all...]
H A Dcm.c232 __be32 local_id; /* Established / timewait */ member
582 static u32 cm_local_id(__be32 local_id) in cm_local_id() argument
584 return (__force u32) (local_id ^ cm.random_id_operand); in cm_local_id()
587 static struct cm_id_private *cm_acquire_id(__be32 local_id, __be32 remote_id) in cm_acquire_id() argument
592 cm_id_priv = xa_load(&cm.local_id_table, cm_local_id(local_id)); in cm_acquire_id()
761 res = cm_acquire_id(timewait_info->work.local_id, in cm_find_remote_id()
866 cm_id_priv->id.local_id = (__force __be32)id ^ cm.random_id_operand; in cm_alloc_id_priv()
881 xa_store(&cm.local_id_table, cm_local_id(cm_id_priv->id.local_id), in cm_finalize_id()
989 static struct cm_timewait_info * cm_create_timewait_info(__be32 local_id) in cm_create_timewait_info() argument
997 timewait_info->work.local_id in cm_create_timewait_info()
[all...]
/kernel/linux/linux-6.6/drivers/infiniband/core/
H A Dcm_trace.h146 __field(unsigned int, local_id)
154 __entry->local_id = be32_to_cpu(cm_id->local_id);
160 TP_printk("local_id=%u remote_id=%u state=%s lap_state=%s",
161 __entry->local_id, __entry->remote_id,
196 __field(u32, local_id)
204 __entry->local_id = be32_to_cpu(cm_id->local_id);
210 TP_printk("local_id=%u remote_id=%u state=%s reason=%s",
211 __entry->local_id, __entr
[all...]
H A Dcm.c188 __be32 local_id; /* Established / timewait */ member
565 static u32 cm_local_id(__be32 local_id) in cm_local_id() argument
567 return (__force u32) (local_id ^ cm.random_id_operand); in cm_local_id()
570 static struct cm_id_private *cm_acquire_id(__be32 local_id, __be32 remote_id) in cm_acquire_id() argument
575 cm_id_priv = xa_load(&cm.local_id_table, cm_local_id(local_id)); in cm_acquire_id()
736 res = cm_acquire_id(timewait_info->work.local_id, in cm_find_remote_id()
835 cm_id_priv->id.local_id = (__force __be32)id ^ cm.random_id_operand; in cm_alloc_id_priv()
850 xa_store(&cm.local_id_table, cm_local_id(cm_id_priv->id.local_id), in cm_finalize_id()
958 static struct cm_timewait_info *cm_create_timewait_info(__be32 local_id) in cm_create_timewait_info() argument
966 timewait_info->work.local_id in cm_create_timewait_info()
[all...]
/kernel/linux/linux-6.6/tools/lib/bpf/
H A Drelo_core.c146 int __bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id, in __bpf_core_types_are_compat() argument
153 local_type = btf_type_by_id(local_btf, local_id); in __bpf_core_types_are_compat()
163 local_type = skip_mods_and_typedefs(local_btf, local_id, &local_id); in __bpf_core_types_are_compat()
185 local_id = local_type->type; in __bpf_core_types_are_compat()
189 local_id = btf_array(local_type)->type; in __bpf_core_types_are_compat()
206 skip_mods_and_typedefs(local_btf, local_p->type, &local_id); in __bpf_core_types_are_compat()
208 err = __bpf_core_types_are_compat(local_btf, local_id, targ_btf, targ_id, in __bpf_core_types_are_compat()
215 skip_mods_and_typedefs(local_btf, local_type->type, &local_id); in __bpf_core_types_are_compat()
221 btf_kind_str(local_type), local_id, targ_i in __bpf_core_types_are_compat()
412 bpf_core_fields_are_compat(const struct btf *local_btf, __u32 local_id, const struct btf *targ_btf, __u32 targ_id) bpf_core_fields_are_compat() argument
491 __u32 local_id; bpf_core_match_member() local
1294 __u32 local_id; bpf_core_calc_relo_insn() local
1544 __bpf_core_types_match(const struct btf *local_btf, __u32 local_id, const struct btf *targ_btf, __u32 targ_id, bool behind_ptr, int level) __bpf_core_types_match() argument
[all...]
H A Drelo_core.h71 int __bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id,
73 int bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id,
75 int __bpf_core_types_match(const struct btf *local_btf, __u32 local_id, const struct btf *targ_btf,
77 int bpf_core_types_match(const struct btf *local_btf, __u32 local_id, const struct btf *targ_btf,
/kernel/linux/linux-5.10/net/mptcp/
H A Dpm.c19 pr_debug("msk=%p, local_id=%d", msk, addr->id); 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()
36 int mptcp_pm_remove_subflow(struct mptcp_sock *msk, u8 local_id) in mptcp_pm_remove_subflow() argument
38 pr_debug("msk=%p, local_id=%d", msk, local_id); in mptcp_pm_remove_subflow()
41 mptcp_pm_nl_rm_subflow_received(msk, local_id); in mptcp_pm_remove_subflow()
H A Dsyncookies.c28 u8 local_id; member
67 entry->local_id = subflow_req->local_id; in mptcp_join_store_state()
H A Dsubflow.c69 int local_id; in subflow_token_join_request() local
77 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request()
78 if (local_id < 0) { in subflow_token_join_request()
82 subflow_req->local_id = local_id; in subflow_token_join_request()
1103 int local_id = loc->id; in __mptcp_subflow_connect() local
1123 if (!local_id) { in __mptcp_subflow_connect()
1128 local_id = err; in __mptcp_subflow_connect()
1147 pr_debug("msk=%p remote_token=%u local_id=%d remote_id=%d", msk, in __mptcp_subflow_connect()
1148 remote_token, local_id, remote_i in __mptcp_subflow_connect()
[all...]
H A Dprotocol.h265 u8 local_id; member
322 u8 local_id; member
456 int mptcp_pm_remove_addr(struct mptcp_sock *msk, u8 local_id);
457 int mptcp_pm_remove_subflow(struct mptcp_sock *msk, u8 local_id);
H A Ddiag.c66 nla_put_u8(skb, MPTCP_SUBFLOW_ATTR_ID_LOC, sf->local_id)) { in subflow_get_info()
/kernel/linux/linux-6.6/drivers/firewire/
H A Dcore-card.c292 int root_id, new_root_id, irm_id, bm_id, local_id; in bm_work() local
327 local_id = card->local_node->node_id; in bm_work()
348 new_root_id = local_id; in bm_work()
355 new_root_id = local_id; in bm_work()
362 transaction_data[1] = cpu_to_be32(local_id); in bm_work()
380 bm_id == 0x3f ? local_id : 0xffc0 | bm_id; in bm_work()
385 if (local_id == irm_id) in bm_work()
410 new_root_id = local_id; in bm_work()
442 new_root_id = local_id; in bm_work()
453 new_root_id = local_id; in bm_work()
[all...]
/kernel/linux/linux-5.10/drivers/firewire/
H A Dcore-card.c292 int root_id, new_root_id, irm_id, bm_id, local_id; in bm_work() local
327 local_id = card->local_node->node_id; in bm_work()
348 new_root_id = local_id; in bm_work()
355 new_root_id = local_id; in bm_work()
362 transaction_data[1] = cpu_to_be32(local_id); in bm_work()
380 bm_id == 0x3f ? local_id : 0xffc0 | bm_id; in bm_work()
385 if (local_id == irm_id) in bm_work()
410 new_root_id = local_id; in bm_work()
437 new_root_id = local_id; in bm_work()
457 new_root_id = local_id; in bm_work()
[all...]
/kernel/linux/linux-5.10/drivers/hwspinlock/
H A Dhwspinlock_internal.h64 int local_id = hwlock - &hwlock->bank->lock[0]; in hwlock_to_id() local
66 return hwlock->bank->base_id + local_id; in hwlock_to_id()
/kernel/linux/linux-6.6/drivers/hwspinlock/
H A Dhwspinlock_internal.h64 int local_id = hwlock - &hwlock->bank->lock[0]; in hwlock_to_id() local
66 return hwlock->bank->base_id + local_id; in hwlock_to_id()
/kernel/linux/linux-6.6/net/mptcp/
H A Dsyncookies.c28 u8 local_id; member
67 entry->local_id = subflow_req->local_id; in mptcp_join_store_state()
H A Dsubflow.c89 int local_id; in subflow_token_join_request() local
97 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request()
98 if (local_id < 0) { in subflow_token_join_request()
102 subflow_req->local_id = local_id; in subflow_token_join_request()
578 static void subflow_set_local_id(struct mptcp_subflow_context *subflow, int local_id) in subflow_set_local_id() argument
580 WARN_ON_ONCE(local_id < 0 || local_id > 255); in subflow_set_local_id()
581 WRITE_ONCE(subflow->local_id, local_id); in subflow_set_local_id()
1515 int local_id = loc->id; __mptcp_subflow_connect() local
[all...]
H A Dprotocol.h420 u8 local_id; member
509 s16 local_id; /* if negative not initialized yet */
560 WRITE_ONCE(subflow->local_id, -1); in mptcp_subflow_ctx_reset()
1014 int local_id = READ_ONCE(subflow->local_id); in subflow_get_local_id() local
1016 if (local_id < 0) in subflow_get_local_id()
1018 return local_id; in subflow_get_local_id()
/kernel/linux/linux-5.10/net/bluetooth/
H A Da2mp.c484 BT_DBG("local_id %d, remote_id %d", req->local_id, req->remote_id); in a2mp_createphyslink_req()
488 rsp.local_id = req->remote_id; in a2mp_createphyslink_req()
489 rsp.remote_id = req->local_id; in a2mp_createphyslink_req()
527 hcon = phylink_add(hdev, mgr, req->local_id, false); in a2mp_createphyslink_req()
565 BT_DBG("local_id %d remote_id %d", req->local_id, req->remote_id); in a2mp_discphyslink_req()
569 rsp.local_id = req->remote_id; in a2mp_discphyslink_req()
570 rsp.remote_id = req->local_id; in a2mp_discphyslink_req()
994 req->local_id in a2mp_send_create_phy_link_req()
[all...]
H A Da2mp.h102 __u8 local_id; member
110 __u8 local_id; member
/kernel/linux/linux-6.6/include/media/
H A Dv4l2-fwnode.h88 * @local_id: identifier of the id this endpoint belongs to
96 unsigned int local_id; member
/kernel/linux/linux-5.10/include/media/
H A Dmedia-entity.h392 * @local_id: next ID, from struct &media_device.id.
394 static inline u32 media_gobj_gen_id(enum media_gobj_type type, u64 local_id) in media_gobj_gen_id() argument
399 id |= local_id & MEDIA_ID_MASK; in media_gobj_gen_id()
H A Dv4l2-fwnode.h145 * @local_id: identifier of the id this endpoint belongs to
153 unsigned int local_id; member
/kernel/linux/linux-5.10/drivers/staging/vt6656/
H A Dkey.c127 if (priv->local_id <= MAC_REVISION_A1) in vnt_set_keys()
/kernel/linux/linux-6.6/drivers/staging/vt6656/
H A Dkey.c125 if (priv->local_id <= MAC_REVISION_A1) in vnt_set_keys()

Completed in 24 milliseconds

123