| /OK3568_Linux_fs/kernel/drivers/net/wireless/mediatek/mt76/ |
| H A D | agg-rx.c | 16 mt76_aggr_release(struct mt76_rx_tid *tid, struct sk_buff_head *frames, int idx) in mt76_aggr_release() argument 20 tid->head = ieee80211_sn_inc(tid->head); in mt76_aggr_release() 22 skb = tid->reorder_buf[idx]; in mt76_aggr_release() 26 tid->reorder_buf[idx] = NULL; in mt76_aggr_release() 27 tid->nframes--; in mt76_aggr_release() 32 mt76_rx_aggr_release_frames(struct mt76_rx_tid *tid, in mt76_rx_aggr_release_frames() argument 38 while (ieee80211_sn_less(tid->head, head)) { in mt76_rx_aggr_release_frames() 39 idx = tid->head % tid->size; in mt76_rx_aggr_release_frames() 40 mt76_aggr_release(tid, frames, idx); in mt76_rx_aggr_release_frames() 45 mt76_rx_aggr_release_head(struct mt76_rx_tid *tid, struct sk_buff_head *frames) in mt76_rx_aggr_release_head() argument [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/core/cuda/ |
| H A D | block.hpp | 90 int tid = flattenedThreadId(); in yota() local 91 value += tid; in yota() 93 for(OutIt t = beg + tid; t < end; t += STRIDE, value += STRIDE) in yota() 134 int tid = flattenedThreadId(); in reduce() local 135 T val = buffer[tid]; in reduce() 137 …if (CTA_SIZE >= 1024) { if (tid < 512) buffer[tid] = val = op(val, buffer[tid + 512]); __syncthrea… in reduce() 138 …if (CTA_SIZE >= 512) { if (tid < 256) buffer[tid] = val = op(val, buffer[tid + 256]); __syncthrea… in reduce() 139 …if (CTA_SIZE >= 256) { if (tid < 128) buffer[tid] = val = op(val, buffer[tid + 128]); __syncthrea… in reduce() 140 …if (CTA_SIZE >= 128) { if (tid < 64) buffer[tid] = val = op(val, buffer[tid + 64]); __syncthrea… in reduce() 142 if (tid < 32) in reduce() [all …]
|
| H A D | warp_reduce.hpp | 55 __device__ __forceinline__ T warp_reduce(volatile T *ptr , const unsigned int tid = threadIdx.x) in warp_reduce() argument 57 const unsigned int lane = tid & 31; // index of thread in warp (0..31) in warp_reduce() 61 T partial = ptr[tid]; in warp_reduce() 63 ptr[tid] = partial = partial + ptr[tid + 16]; in warp_reduce() 64 ptr[tid] = partial = partial + ptr[tid + 8]; in warp_reduce() 65 ptr[tid] = partial = partial + ptr[tid + 4]; in warp_reduce() 66 ptr[tid] = partial = partial + ptr[tid + 2]; in warp_reduce() 67 ptr[tid] = partial = partial + ptr[tid + 1]; in warp_reduce() 70 return ptr[tid - lane]; in warp_reduce()
|
| H A D | scan.hpp | 83 __device__ __forceinline__ unsigned int index(const unsigned int tid) in index() 85 return tid; in index() 117 __device__ __forceinline__ unsigned int index(const unsigned int tid) in index() 119 return (tid >> warp_log) * warp_smem_stride + 16 + (tid & warp_mask); in index() 142 const unsigned int tid = threadIdx.x; in operator ()() local 143 const unsigned int lane = tid & warp_mask; in operator ()() 144 const unsigned int warp = tid >> warp_log; in operator ()() 148 const unsigned int idx = scan.index(tid); in operator ()() 180 __device__ T warpScanInclusive(T idata, volatile T* s_Data, unsigned int tid) in warpScanInclusive() argument 196 unsigned int pos = 2 * tid - (tid & (OPENCV_CUDA_WARP_SIZE - 1)); in warpScanInclusive() [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/cuda/ |
| H A D | block.hpp | 90 int tid = flattenedThreadId(); in yota() local 91 value += tid; in yota() 93 for(OutIt t = beg + tid; t < end; t += STRIDE, value += STRIDE) in yota() 134 int tid = flattenedThreadId(); in reduce() local 135 T val = buffer[tid]; in reduce() 137 …if (CTA_SIZE >= 1024) { if (tid < 512) buffer[tid] = val = op(val, buffer[tid + 512]); __syncthrea… in reduce() 138 …if (CTA_SIZE >= 512) { if (tid < 256) buffer[tid] = val = op(val, buffer[tid + 256]); __syncthrea… in reduce() 139 …if (CTA_SIZE >= 256) { if (tid < 128) buffer[tid] = val = op(val, buffer[tid + 128]); __syncthrea… in reduce() 140 …if (CTA_SIZE >= 128) { if (tid < 64) buffer[tid] = val = op(val, buffer[tid + 64]); __syncthrea… in reduce() 142 if (tid < 32) in reduce() [all …]
|
| H A D | warp_reduce.hpp | 55 __device__ __forceinline__ T warp_reduce(volatile T *ptr , const unsigned int tid = threadIdx.x) in warp_reduce() argument 57 const unsigned int lane = tid & 31; // index of thread in warp (0..31) in warp_reduce() 61 T partial = ptr[tid]; in warp_reduce() 63 ptr[tid] = partial = partial + ptr[tid + 16]; in warp_reduce() 64 ptr[tid] = partial = partial + ptr[tid + 8]; in warp_reduce() 65 ptr[tid] = partial = partial + ptr[tid + 4]; in warp_reduce() 66 ptr[tid] = partial = partial + ptr[tid + 2]; in warp_reduce() 67 ptr[tid] = partial = partial + ptr[tid + 1]; in warp_reduce() 70 return ptr[tid - lane]; in warp_reduce()
|
| H A D | scan.hpp | 83 __device__ __forceinline__ unsigned int index(const unsigned int tid) in index() 85 return tid; in index() 117 __device__ __forceinline__ unsigned int index(const unsigned int tid) in index() 119 return (tid >> warp_log) * warp_smem_stride + 16 + (tid & warp_mask); in index() 142 const unsigned int tid = threadIdx.x; in operator ()() local 143 const unsigned int lane = tid & warp_mask; in operator ()() 144 const unsigned int warp = tid >> warp_log; in operator ()() 148 const unsigned int idx = scan.index(tid); in operator ()() 180 __device__ T warpScanInclusive(T idata, volatile T* s_Data, unsigned int tid) in warpScanInclusive() argument 196 unsigned int pos = 2 * tid - (tid & (OPENCV_CUDA_WARP_SIZE - 1)); in warpScanInclusive() [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/core/cuda/ |
| H A D | block.hpp | 90 int tid = flattenedThreadId(); in yota() local 91 value += tid; in yota() 93 for(OutIt t = beg + tid; t < end; t += STRIDE, value += STRIDE) in yota() 134 int tid = flattenedThreadId(); in reduce() local 135 T val = buffer[tid]; in reduce() 137 …if (CTA_SIZE >= 1024) { if (tid < 512) buffer[tid] = val = op(val, buffer[tid + 512]); __syncthrea… in reduce() 138 …if (CTA_SIZE >= 512) { if (tid < 256) buffer[tid] = val = op(val, buffer[tid + 256]); __syncthrea… in reduce() 139 …if (CTA_SIZE >= 256) { if (tid < 128) buffer[tid] = val = op(val, buffer[tid + 128]); __syncthrea… in reduce() 140 …if (CTA_SIZE >= 128) { if (tid < 64) buffer[tid] = val = op(val, buffer[tid + 64]); __syncthrea… in reduce() 142 if (tid < 32) in reduce() [all …]
|
| H A D | warp_reduce.hpp | 55 __device__ __forceinline__ T warp_reduce(volatile T *ptr , const unsigned int tid = threadIdx.x) in warp_reduce() argument 57 const unsigned int lane = tid & 31; // index of thread in warp (0..31) in warp_reduce() 61 T partial = ptr[tid]; in warp_reduce() 63 ptr[tid] = partial = partial + ptr[tid + 16]; in warp_reduce() 64 ptr[tid] = partial = partial + ptr[tid + 8]; in warp_reduce() 65 ptr[tid] = partial = partial + ptr[tid + 4]; in warp_reduce() 66 ptr[tid] = partial = partial + ptr[tid + 2]; in warp_reduce() 67 ptr[tid] = partial = partial + ptr[tid + 1]; in warp_reduce() 70 return ptr[tid - lane]; in warp_reduce()
|
| H A D | scan.hpp | 83 __device__ __forceinline__ unsigned int index(const unsigned int tid) in index() 85 return tid; in index() 117 __device__ __forceinline__ unsigned int index(const unsigned int tid) in index() 119 return (tid >> warp_log) * warp_smem_stride + 16 + (tid & warp_mask); in index() 142 const unsigned int tid = threadIdx.x; in operator ()() local 143 const unsigned int lane = tid & warp_mask; in operator ()() 144 const unsigned int warp = tid >> warp_log; in operator ()() 148 const unsigned int idx = scan.index(tid); in operator ()() 180 __device__ T warpScanInclusive(T idata, volatile T* s_Data, unsigned int tid) in warpScanInclusive() argument 196 unsigned int pos = 2 * tid - (tid & (OPENCV_CUDA_WARP_SIZE - 1)); in warpScanInclusive() [all …]
|
| /OK3568_Linux_fs/kernel/net/mac80211/ |
| H A D | agg-tx.c | 62 const u8 *da, u16 tid, in ieee80211_send_addba_request() argument 100 capab |= (u16)(tid << 2); /* bit 5:2 TID number */ in ieee80211_send_addba_request() 109 ieee80211_tx_skb_tid(sdata, skb, tid); in ieee80211_send_addba_request() 112 void ieee80211_send_bar(struct ieee80211_vif *vif, u8 *ra, u16 tid, u16 ssn) in ieee80211_send_bar() argument 132 bar_control |= (u16)(tid << IEEE80211_BAR_CTRL_TID_INFO_SHIFT); in ieee80211_send_bar() 138 ieee80211_tx_skb_tid(sdata, skb, tid); in ieee80211_send_bar() 142 void ieee80211_assign_tid_tx(struct sta_info *sta, int tid, in ieee80211_assign_tid_tx() argument 147 rcu_assign_pointer(sta->ampdu_mlme.tid_tx[tid], tid_tx); in ieee80211_assign_tid_tx() 162 ieee80211_stop_queue_agg(struct ieee80211_sub_if_data *sdata, int tid) in __acquires() 164 int queue = sdata->vif.hw_queue[ieee80211_ac_from_tid(tid)]; in __acquires() [all …]
|
| H A D | agg-rx.c | 58 void ___ieee80211_stop_rx_ba_session(struct sta_info *sta, u16 tid, in ___ieee80211_stop_rx_ba_session() argument 66 .tid = tid, in ___ieee80211_stop_rx_ba_session() 74 tid_rx = rcu_dereference_protected(sta->ampdu_mlme.tid_rx[tid], in ___ieee80211_stop_rx_ba_session() 77 if (!test_bit(tid, sta->ampdu_mlme.agg_session_valid)) in ___ieee80211_stop_rx_ba_session() 80 RCU_INIT_POINTER(sta->ampdu_mlme.tid_rx[tid], NULL); in ___ieee80211_stop_rx_ba_session() 81 __clear_bit(tid, sta->ampdu_mlme.agg_session_valid); in ___ieee80211_stop_rx_ba_session() 85 sta->sta.addr, tid, in ___ieee80211_stop_rx_ba_session() 92 sta->sta.addr, tid); in ___ieee80211_stop_rx_ba_session() 97 tid, WLAN_BACK_RECIPIENT, reason); in ___ieee80211_stop_rx_ba_session() 117 void __ieee80211_stop_rx_ba_session(struct sta_info *sta, u16 tid, in __ieee80211_stop_rx_ba_session() argument [all …]
|
| /OK3568_Linux_fs/kernel/fs/cifs/ |
| H A D | trace.h | 19 __u32 tid, 24 TP_ARGS(xid, fid, tid, sesid, offset, len, rc), 28 __field(__u32, tid) 37 __entry->tid = tid; 44 __entry->xid, __entry->sesid, __entry->tid, __entry->fid, 52 __u32 tid, \ 57 TP_ARGS(xid, fid, tid, sesid, offset, len, rc)) 70 __u32 tid, 74 TP_ARGS(xid, fid, tid, sesid, offset, len), 78 __field(__u32, tid) [all …]
|
| /OK3568_Linux_fs/kernel/drivers/net/ethernet/marvell/mvpp2/ |
| H A D | mvpp2_prs.c | 47 int tid) in mvpp2_prs_init_from_hw() argument 51 if (tid > MVPP2_PRS_TCAM_SRAM_SIZE - 1) in mvpp2_prs_init_from_hw() 55 pe->index = tid; in mvpp2_prs_init_from_hw() 367 int tid; in mvpp2_prs_flow_find() local 370 for (tid = MVPP2_PRS_TCAM_SRAM_SIZE - 1; tid >= 0; tid--) { in mvpp2_prs_flow_find() 373 if (!priv->prs_shadow[tid].valid || in mvpp2_prs_flow_find() 374 priv->prs_shadow[tid].lu != MVPP2_PRS_LU_FLOWS) in mvpp2_prs_flow_find() 377 mvpp2_prs_init_from_hw(priv, &pe, tid); in mvpp2_prs_flow_find() 382 return tid; in mvpp2_prs_flow_find() 392 int tid; in mvpp2_prs_tcam_first_free() local [all …]
|
| /OK3568_Linux_fs/yocto/poky/bitbake/lib/bb/ |
| H A D | runqueue.py | 35 def fn_from_tid(tid): argument 36 return tid.rsplit(":", 1)[0] 38 def taskname_from_tid(tid): argument 39 return tid.rsplit(":", 1)[1] 41 def mc_from_tid(tid): argument 42 if tid.startswith('mc:') and tid.count(':') >= 2: 43 return tid.split(':')[1] 46 def split_tid(tid): argument 47 (mc, fn, taskname, _) = split_tid_mcfn(tid) 56 def split_tid_mcfn(tid): argument [all …]
|
| H A D | siggen.py | 78 def get_unihash(self, tid): argument 79 return self.taskhash[tid] 81 def prep_taskhash(self, tid, deps, dataCaches): argument 84 def get_taskhash(self, tid, deps, dataCaches): argument 85 self.taskhash[tid] = hashlib.sha256(tid.encode("utf-8")).hexdigest() 86 return self.taskhash[tid] 209 tid = fn + ":" + task 210 if not ignore_mismatch and tid in self.basehash and self.basehash[tid] != basehash[tid]: 211 …adata is not deterministic and this needs to be fixed." % (tid, self.basehash[tid], basehash[tid])) 218 self.basehash[tid] = basehash[tid] [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/cuda/detail/ |
| H A D | reduce.hpp | 74 … static __device__ void loadToSmem(const PointerTuple& smem, const ValTuple& val, unsigned int tid) in loadToSmem() 76 thrust::get<I>(smem)[tid] = thrust::get<I>(val); in loadToSmem() 78 For<I + 1, N>::loadToSmem(smem, val, tid); in loadToSmem() 81 …tatic __device__ void loadFromSmem(const PointerTuple& smem, const ValTuple& val, unsigned int tid) in loadFromSmem() 83 thrust::get<I>(val) = thrust::get<I>(smem)[tid]; in loadFromSmem() 85 For<I + 1, N>::loadFromSmem(smem, val, tid); in loadFromSmem() 89 …e__ void merge(const PointerTuple& smem, const ValTuple& val, unsigned int tid, unsigned int delta… in merge() 91 …pename thrust::tuple_element<I, PointerTuple>::type>::type reg = thrust::get<I>(smem)[tid + delta]; in merge() 92 … thrust::get<I>(smem)[tid] = thrust::get<I>(val) = thrust::get<I>(op)(thrust::get<I>(val), reg); in merge() 94 For<I + 1, N>::merge(smem, val, tid, delta, op); in merge() [all …]
|
| H A D | reduce_key_val.hpp | 74 … __device__ void loadToSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned int tid) in loadToSmem() 76 thrust::get<I>(smem)[tid] = thrust::get<I>(data); in loadToSmem() 78 For<I + 1, N>::loadToSmem(smem, data, tid); in loadToSmem() 81 …_device__ void loadFromSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned int tid) in loadFromSmem() 83 thrust::get<I>(data) = thrust::get<I>(smem)[tid]; in loadFromSmem() 85 For<I + 1, N>::loadFromSmem(smem, data, tid); in loadFromSmem() 96 …id copy(const PointerTuple& svals, const ReferenceTuple& val, unsigned int tid, unsigned int delta) in copy() 98 … thrust::get<I>(svals)[tid] = thrust::get<I>(val) = thrust::get<I>(svals)[tid + delta]; in copy() 100 For<I + 1, N>::copy(svals, val, tid, delta); in copy() 120 unsigned int tid, unsigned int delta) in merge() [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/core/cuda/detail/ |
| H A D | reduce.hpp | 74 … static __device__ void loadToSmem(const PointerTuple& smem, const ValTuple& val, unsigned int tid) in loadToSmem() 76 thrust::get<I>(smem)[tid] = thrust::get<I>(val); in loadToSmem() 78 For<I + 1, N>::loadToSmem(smem, val, tid); in loadToSmem() 81 …tatic __device__ void loadFromSmem(const PointerTuple& smem, const ValTuple& val, unsigned int tid) in loadFromSmem() 83 thrust::get<I>(val) = thrust::get<I>(smem)[tid]; in loadFromSmem() 85 For<I + 1, N>::loadFromSmem(smem, val, tid); in loadFromSmem() 89 …e__ void merge(const PointerTuple& smem, const ValTuple& val, unsigned int tid, unsigned int delta… in merge() 91 …pename thrust::tuple_element<I, PointerTuple>::type>::type reg = thrust::get<I>(smem)[tid + delta]; in merge() 92 … thrust::get<I>(smem)[tid] = thrust::get<I>(val) = thrust::get<I>(op)(thrust::get<I>(val), reg); in merge() 94 For<I + 1, N>::merge(smem, val, tid, delta, op); in merge() [all …]
|
| H A D | reduce_key_val.hpp | 74 … __device__ void loadToSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned int tid) in loadToSmem() 76 thrust::get<I>(smem)[tid] = thrust::get<I>(data); in loadToSmem() 78 For<I + 1, N>::loadToSmem(smem, data, tid); in loadToSmem() 81 …_device__ void loadFromSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned int tid) in loadFromSmem() 83 thrust::get<I>(data) = thrust::get<I>(smem)[tid]; in loadFromSmem() 85 For<I + 1, N>::loadFromSmem(smem, data, tid); in loadFromSmem() 96 …id copy(const PointerTuple& svals, const ReferenceTuple& val, unsigned int tid, unsigned int delta) in copy() 98 … thrust::get<I>(svals)[tid] = thrust::get<I>(val) = thrust::get<I>(svals)[tid + delta]; in copy() 100 For<I + 1, N>::copy(svals, val, tid, delta); in copy() 120 unsigned int tid, unsigned int delta) in merge() [all …]
|
| /OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/core/cuda/detail/ |
| H A D | reduce.hpp | 74 … static __device__ void loadToSmem(const PointerTuple& smem, const ValTuple& val, unsigned int tid) in loadToSmem() 76 thrust::get<I>(smem)[tid] = thrust::get<I>(val); in loadToSmem() 78 For<I + 1, N>::loadToSmem(smem, val, tid); in loadToSmem() 81 …tatic __device__ void loadFromSmem(const PointerTuple& smem, const ValTuple& val, unsigned int tid) in loadFromSmem() 83 thrust::get<I>(val) = thrust::get<I>(smem)[tid]; in loadFromSmem() 85 For<I + 1, N>::loadFromSmem(smem, val, tid); in loadFromSmem() 89 …e__ void merge(const PointerTuple& smem, const ValTuple& val, unsigned int tid, unsigned int delta… in merge() 91 …pename thrust::tuple_element<I, PointerTuple>::type>::type reg = thrust::get<I>(smem)[tid + delta]; in merge() 92 … thrust::get<I>(smem)[tid] = thrust::get<I>(val) = thrust::get<I>(op)(thrust::get<I>(val), reg); in merge() 94 For<I + 1, N>::merge(smem, val, tid, delta, op); in merge() [all …]
|
| H A D | reduce_key_val.hpp | 74 … __device__ void loadToSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned int tid) in loadToSmem() 76 thrust::get<I>(smem)[tid] = thrust::get<I>(data); in loadToSmem() 78 For<I + 1, N>::loadToSmem(smem, data, tid); in loadToSmem() 81 …_device__ void loadFromSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned int tid) in loadFromSmem() 83 thrust::get<I>(data) = thrust::get<I>(smem)[tid]; in loadFromSmem() 85 For<I + 1, N>::loadFromSmem(smem, data, tid); in loadFromSmem() 96 …id copy(const PointerTuple& svals, const ReferenceTuple& val, unsigned int tid, unsigned int delta) in copy() 98 … thrust::get<I>(svals)[tid] = thrust::get<I>(val) = thrust::get<I>(svals)[tid + delta]; in copy() 100 For<I + 1, N>::copy(svals, val, tid, delta); in copy() 120 unsigned int tid, unsigned int delta) in merge() [all …]
|
| /OK3568_Linux_fs/kernel/fs/jfs/ |
| H A D | namei.c | 66 tid_t tid; /* transaction id */ in jfs_create() local 98 tid = txBegin(dip->i_sb, 0); in jfs_create() 103 rc = jfs_init_acl(tid, ip, dip); in jfs_create() 107 rc = jfs_init_security(tid, ip, dip, &dentry->d_name); in jfs_create() 109 txAbort(tid, 0); in jfs_create() 115 txAbort(tid, 0); in jfs_create() 119 tblk = tid_to_tblock(tid); in jfs_create() 130 xtInitRoot(tid, ip); in jfs_create() 137 if ((rc = dtInsert(tid, dip, &dname, &ino, &btstack))) { in jfs_create() 140 txAbort(tid, 1); /* Marks Filesystem dirty */ in jfs_create() [all …]
|
| /OK3568_Linux_fs/kernel/tools/perf/scripts/python/ |
| H A D | futex-contention.py | 29 def syscalls__sys_enter_futex(event, ctxt, cpu, s, ns, tid, comm, callchain, argument 35 process_names[tid] = comm 36 thread_thislock[tid] = uaddr 37 thread_blocktime[tid] = nsecs(s, ns) 40 def syscalls__sys_exit_futex(event, ctxt, cpu, s, ns, tid, comm, callchain, argument 42 if tid in thread_blocktime: 43 elapsed = nsecs(s, ns) - thread_blocktime[tid] 44 add_stats(lock_waits, (tid, thread_thislock[tid]), elapsed) 45 del thread_blocktime[tid] 46 del thread_thislock[tid] [all …]
|
| /OK3568_Linux_fs/external/rkwifibt/drivers/rtl8852bs/phl/ |
| H A D | phl_rx_agg.c | 114 u16 tid) in rtw_phl_stop_rx_ba_session() argument 128 PHL_INFO("Stop rx BA session for sta=0x%p, tid=%u\n", sta, tid); in rtw_phl_stop_rx_ba_session() 129 rtw_hal_stop_ba_session(phl_info->hal, sta, tid); in rtw_phl_stop_rx_ba_session() 131 if (tid >= ARRAY_SIZE(sta->tid_rx)) in rtw_phl_stop_rx_ba_session() 135 if (!sta->tid_rx[tid]) { in rtw_phl_stop_rx_ba_session() 140 r = sta->tid_rx[tid]; in rtw_phl_stop_rx_ba_session() 141 sta->tid_rx[tid] = NULL; in rtw_phl_stop_rx_ba_session() 150 PHL_INFO("Rx BA session for sta=0x%p, tid=%u freed\n", sta, tid); in rtw_phl_stop_rx_ba_session() 155 u16 timeout, u16 ssn, u16 tid, in phl_tid_ampdu_rx_alloc() argument 198 r->tid = tid; in phl_tid_ampdu_rx_alloc() [all …]
|