Lines Matching defs:Packet
742 hsa_kernel_dispatch_packet_t *Packet = acquirePacket(PacketId);
743 assert(Packet && "Invalid packet");
751 Packet->workgroup_size_x = NumThreads[0];
752 Packet->workgroup_size_y = NumThreads[1];
753 Packet->workgroup_size_z = NumThreads[2];
754 Packet->reserved0 = 0;
755 Packet->grid_size_x = NumBlocks[0] * NumThreads[0];
756 Packet->grid_size_y = NumBlocks[1] * NumThreads[1];
757 Packet->grid_size_z = NumBlocks[2] * NumThreads[2];
758 Packet->private_segment_size =
760 Packet->group_segment_size = GroupSize;
761 Packet->kernel_object = Kernel.getKernelObject();
762 Packet->kernarg_address = KernelArgs;
763 Packet->reserved2 = 0;
764 Packet->completion_signal = OutputSignal->get();
767 publishKernelPacket(PacketId, Setup, Packet);
794 hsa_barrier_and_packet_t *Packet =
796 assert(Packet && "Invalid packet");
798 Packet->reserved0 = 0;
799 Packet->reserved1 = 0;
800 Packet->dep_signal[0] = {0};
801 Packet->dep_signal[1] = {0};
802 Packet->dep_signal[2] = {0};
803 Packet->dep_signal[3] = {0};
804 Packet->dep_signal[4] = {0};
805 Packet->reserved2 = 0;
806 Packet->completion_signal = {0};
810 Packet->completion_signal = OutputSignal->get();
812 Packet->dep_signal[0] = InputSignal1->get();
814 Packet->dep_signal[1] = InputSignal2->get();
817 publishBarrierPacket(PacketId, Packet);
845 hsa_kernel_dispatch_packet_t *Packet) {
846 uint32_t *PacketPtr = reinterpret_cast<uint32_t *>(Packet);
864 hsa_barrier_and_packet_t *Packet) {
865 uint32_t *PacketPtr = reinterpret_cast<uint32_t *>(Packet);