1404   struct GOMP_kernel_launch_attributes *kla;  in parse_target_attributes()  local
1405   kla = (struct GOMP_kernel_launch_attributes *) *input;  in parse_target_attributes()
1406   *result = kla;  in parse_target_attributes()
1407   if (kla->ndim == 0 || kla->ndim > 3)  in parse_target_attributes()
1408     GOMP_PLUGIN_fatal ("Invalid number of dimensions (%u)", kla->ndim);  in parse_target_attributes()
1410   HSA_DEBUG ("GOMP_OFFLOAD_run called with %u dimensions:\n", kla->ndim);  in parse_target_attributes()
1412   for (i = 0; i < kla->ndim; i++)  in parse_target_attributes()
1415 		 kla->gdims[i], kla->wdims[i]);  in parse_target_attributes()
1416       if (kla->gdims[i] == 0)  in parse_target_attributes()
1482 	    struct GOMP_kernel_launch_attributes *kla)  in run_kernel()  argument
1517   packet->grid_size_x = kla->gdims[0];  in run_kernel()
1518   packet->workgroup_size_x = get_group_size (kla->ndim, kla->gdims[0],  in run_kernel()
1519 					     kla->wdims[0]);  in run_kernel()
1521   if (kla->ndim >= 2)  in run_kernel()
1523       packet->grid_size_y = kla->gdims[1];  in run_kernel()
1524       packet->workgroup_size_y = get_group_size (kla->ndim, kla->gdims[1],  in run_kernel()
1525 						 kla->wdims[1]);  in run_kernel()
1533   if (kla->ndim == 3)  in run_kernel()
1535       packet->grid_size_z = kla->gdims[2];  in run_kernel()
1536       packet->workgroup_size_z = get_group_size (kla->ndim, kla->gdims[2],  in run_kernel()
1537 					     kla->wdims[2]);  in run_kernel()
1576 			(uint16_t) kla->ndim << HSA_KERNEL_DISPATCH_PACKET_SETUP_DIMENSIONS);  in run_kernel()
1620   struct GOMP_kernel_launch_attributes *kla;  in GOMP_OFFLOAD_run()  local
1621   if (!parse_target_attributes (args, &def, &kla))  in GOMP_OFFLOAD_run()
1626   run_kernel (kernel, vars, kla);  in GOMP_OFFLOAD_run()