remove cq lock (#357)

[ROCm/rocshmem commit: b28a56bd54]
This commit is contained in:
Yiltan
2025-12-15 09:23:24 -05:00
کامیت شده توسط GitHub
والد 5e2ba952f3
کامیت 43363894a8
2فایلهای تغییر یافته به همراه1 افزوده شده و 8 حذف شده
@@ -39,10 +39,6 @@ struct bnxt_device_wq {
uint32_t tail;
uint32_t flags;
uint32_t id;
uint32_t lock;
uint32_t db_cnt {0};
} __attribute__((packed));
struct bnxt_device_cq : public bnxt_device_wq {
@@ -56,6 +52,7 @@ struct bnxt_device_sq : public bnxt_device_wq {
uint32_t msn_tbl_sz;
uint32_t psn_sz_log2;
uint64_t mtu;
uint32_t lock;
} __attribute__((packed));
struct bnxt_host_cq {
@@ -177,8 +177,6 @@ __device__ void QueuePair::poll_cq_until(uint32_t requested_available_slots) {
sq_depth = sq.depth;
aquire_lock(&cq.lock);
do {
cqe = (struct bnxt_re_req_cqe *) cq.buf;
@@ -197,8 +195,6 @@ __device__ void QueuePair::poll_cq_until(uint32_t requested_available_slots) {
consumed_slots = (sq_tail - sq_head + sq_depth) % sq_depth;
available_slots = sq_depth - consumed_slots;
} while (available_slots < requested_available_slots);
release_lock(&cq.lock);
}
__device__ void QueuePair::bnxt_quiet() {