From nobody Sun Oct 5 05:29:01 2025 Received: from AM0PR83CU005.outbound.protection.outlook.com (mail-westeuropeazon11010023.outbound.protection.outlook.com [52.101.69.23]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id CCB4649641 for ; Thu, 7 Aug 2025 16:27:36 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=fail smtp.client-ip=52.101.69.23 ARC-Seal: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584061; cv=fail; b=WbfD/rVkDx3lE/3GrYTRO0VDdN3Ax8C3lZt9InSeyiR6Pgs4hHcdKjxrK6eQp9Owjz17xn4n/SHdtgbAZNFHWM/8F6i52EWbJI1N5jUToxDbQXD+ELGEl+uIcH9PNOIhuB9DnEEvl1a5HFeDUukYRaNATE9BxMgVGar1XyYj8BU= ARC-Message-Signature: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584061; c=relaxed/simple; bh=IyPMFilGqS4MA+Q9Cwnft4hbs7bv0U8AyC83EE9h4mc=; h=From:To:Cc:Subject:Date:Message-ID:In-Reply-To:References: Content-Type:MIME-Version; b=AMPjG2QhF3eeK4BCEuGlSq/mUPtJeqwcrL84vqB1oZS7UJBz0b/TpgXnln8UM9Psc5nI7AfkqH9/jmTBohM5AzpTeTjNTWlBZ9/t63P7aGhFnb+OaRbmaBIEKuv2X7E6dCCC14j5qTKh0AO1koEhnkRGmIUSzz2juDm9zSXBJmI= ARC-Authentication-Results: i=3; smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com; spf=pass smtp.mailfrom=arm.com; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=qUHUelaM; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=qUHUelaM; arc=fail smtp.client-ip=52.101.69.23 Authentication-Results: smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com Authentication-Results: smtp.subspace.kernel.org; spf=pass smtp.mailfrom=arm.com Authentication-Results: smtp.subspace.kernel.org; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="qUHUelaM"; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="qUHUelaM" ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=xboalKXIhLR8xRGzj6MiWO3BIq5/lySk+KrD+MUk4GaxVLTN57gZ4+TeHAAdxrK7Bf0MEhIZr/DXAyO2/7KtxhEf8Nf12agQi3AiuBdB/ScNIetVkjlzEwhbJwhF1V/RWbSsTJ6Ffi8p+4IPNvkYcBfAv+iFkOTOTbkbJFl79c+Mc2SvPTv6ksqKZDcQZuO76of/VoUSQsd9Nohcyx8CqN2+/S4t0r4jOshRUp0bi4rvC/3DW7+n+4v7++6UQ3wUClIMNdqmGeG/VjtVlgSqPSgKziEFgn5aEUz4e4LyOe3otwkuNbMF1NSikNGk9BHHKw49WjSh7P8N3Q1FfOjx2g== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=h+G6jj668AdE7CkGyJ1kq5ZjJKQBUGx1RaErErL/EeE=; b=NmbirHDARtFSDCJTth1aP5D7Ir+A0wHf7M4K8nMFv46yozYyjHTGKfp+SLDRJvw+/Y0qAC8ZShPExAuYWxPPZLzf1BdvGw17cX6Li5tvh5lTNPg5DR5OruEdTeyytCEKczy1VFpGAFZQRryLEIKwfInzo8kc5pJ/p0XLtQXz6jPoA8kKiZR7HJdqAlHxbDXgHfVuohdxd4kwzcgjHv9+P6LpR9oB3Pdewc39Prnhxdfe3kfO9jI/fiftts3OcS6hcZf+HDf/fmXt+pPOCbcgs9X2rJrYPxEzN0EylQ+kl9sE11dp/UMaWcdXi3CHOgcFHsyAR88u6odm/wR4Z4ogBQ== ARC-Authentication-Results: i=2; mx.microsoft.com 1; spf=pass (sender ip is 4.158.2.129) smtp.rcpttodomain=lists.freedesktop.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=pass (signature was verified) header.d=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=h+G6jj668AdE7CkGyJ1kq5ZjJKQBUGx1RaErErL/EeE=; b=qUHUelaMvopOaWMht/k0Yy29ZCfFCyAA2tnDgLKMGcVbSYDoVzhCWuFRJmoV8TEC4C9hHtqH9DhGcFyCl6uE6+lzlphUmaGyaMxO/CLWMRxRRoZkEs7afUq0DiQM2L7S1iDoxs247FHVTEcDi2suphjKY0zv5JgyfAJkbc7mmdE= Received: from AM8P191CA0016.EURP191.PROD.OUTLOOK.COM (2603:10a6:20b:21a::21) by AS8PR08MB6056.eurprd08.prod.outlook.com (2603:10a6:20b:299::18) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.14; Thu, 7 Aug 2025 16:27:31 +0000 Received: from AM4PEPF00025F9A.EURPRD83.prod.outlook.com (2603:10a6:20b:21a:cafe::7a) by AM8P191CA0016.outlook.office365.com (2603:10a6:20b:21a::21) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.16 via Frontend Transport; Thu, 7 Aug 2025 16:27:31 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 4.158.2.129) smtp.mailfrom=arm.com; dkim=pass (signature was verified) header.d=arm.com;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 4.158.2.129 as permitted sender) receiver=protection.outlook.com; client-ip=4.158.2.129; helo=outbound-uk1.az.dlp.m.darktrace.com; pr=C Received: from outbound-uk1.az.dlp.m.darktrace.com (4.158.2.129) by AM4PEPF00025F9A.mail.protection.outlook.com (10.167.16.9) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9031.0 via Frontend Transport; Thu, 7 Aug 2025 16:27:30 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=nzWiUGOWInhV6KkchLrXTrLOXfvXqH0yrBN8aid8k+ZZl1l1IKQfU8UXTUyIh4l/MKbiYHGN73kHzvFolRQBx+9P45VmjufNQNrMueTOolIyIrZno21MXulUuBw0xTljc+mDMgnP6xO/0zL3sVAyigxQe6gHqUfjNf7Lr9EGH3i2PS8UDcN2WhSn1EA6oKWIqvcGFXSzTdbcCxavi+s1Yr5eCfF8vuarh7B5IM/5VXuoCtrRYEEaW6ELrcrJJUyttsz6B4nhjZPttWtuEesniZdWEloft2Tr3wUBcwtZIlOt6BYsKTFut/8degyQfClPk1G1YNzSQmEOTxt0Hd2hLA== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=h+G6jj668AdE7CkGyJ1kq5ZjJKQBUGx1RaErErL/EeE=; b=aKUJOQCKAjcbO3+jDiE9v28nGrciEJiqmRtjnzSUU58J9UQN4tMeKGJ8UpDWsYZcEeguXBzycvQlYvdCU3c54MAvUV7C4aHNpwOzRzi71vz5FcF8uxYSxwfeg6n6e9gX+3WWuOpgUfAysZmARatHI7k23r/nlDmaTzZNIrIaEr2FJvrD7mT1Q6fve3JJWcovQkdVqBcfo/RPMLS7AChX+aqyIegxwHybDKVJ4tfgzoQCB7GP+pxPuwEKJMXxGSScH4vF6qzyBbWn6neHCkEc/IUlnreSt6iR+eLDmCAhDV6M66KIl69A44FhQixwmzDbxcA+hzaPJdoO4w3Bud4+ag== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=h+G6jj668AdE7CkGyJ1kq5ZjJKQBUGx1RaErErL/EeE=; b=qUHUelaMvopOaWMht/k0Yy29ZCfFCyAA2tnDgLKMGcVbSYDoVzhCWuFRJmoV8TEC4C9hHtqH9DhGcFyCl6uE6+lzlphUmaGyaMxO/CLWMRxRRoZkEs7afUq0DiQM2L7S1iDoxs247FHVTEcDi2suphjKY0zv5JgyfAJkbc7mmdE= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) by DB9PR08MB9443.eurprd08.prod.outlook.com (2603:10a6:10:45b::19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.13; Thu, 7 Aug 2025 16:26:59 +0000 Received: from VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74]) by VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74%5]) with mapi id 15.20.9009.016; Thu, 7 Aug 2025 16:26:59 +0000 From: Karunika Choo To: dri-devel@lists.freedesktop.org Cc: nd@arm.com, Boris Brezillon , Steven Price , Liviu Dudau , Maarten Lankhorst , Maxime Ripard , Thomas Zimmermann , David Airlie , Simona Vetter , linux-kernel@vger.kernel.org, Chia-I Wu Subject: [PATCH v9 1/7] drm/panthor: Add panthor_hw and move gpu_info initialization into it Date: Thu, 7 Aug 2025 17:26:27 +0100 Message-ID: <20250807162633.3666310-2-karunika.choo@arm.com> X-Mailer: git-send-email 2.49.0 In-Reply-To: <20250807162633.3666310-1-karunika.choo@arm.com> References: <20250807162633.3666310-1-karunika.choo@arm.com> Content-Transfer-Encoding: quoted-printable X-ClientProxiedBy: LO4P123CA0623.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:294::18) To VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) Precedence: bulk X-Mailing-List: linux-kernel@vger.kernel.org List-Id: List-Subscribe: List-Unsubscribe: MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: VI0PR08MB11200:EE_|DB9PR08MB9443:EE_|AM4PEPF00025F9A:EE_|AS8PR08MB6056:EE_ X-MS-Office365-Filtering-Correlation-Id: e7018b97-c139-4add-beb0-08ddd5cf4e9a X-LD-Processed: f34e5979-57d9-4aaa-ad4d-b122a662184d,ExtAddr,ExtAddr x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|376014|366016|1800799024; X-Microsoft-Antispam-Message-Info-Original: =?us-ascii?Q?4CZ9us7cNC65NZsYh+TLOvC97lUszLKlmmkNr8ny2ppHGV/68IXTK+fMu1KZ?= =?us-ascii?Q?OBMl4kR4KpuVnv+ne05nUmfB11KlJLlghLIyMwSqMSghID0hMXuq6M0l2AzG?= =?us-ascii?Q?RsBJWfgaeaCeyerMnyuUO3ha0Ox43gaZJM6i8q6Gfxav+50tP8FFNHrlXTE6?= =?us-ascii?Q?c0h9DMmPgze9P+NOrf8rVI/DDPH3XVX09WV9eFleZGw8qW8BchGlzVAyjbr2?= =?us-ascii?Q?P4clcBbK1uoRqvbks4RsjwPzvmyu4dRHTsXg1qIAv5OTZeSeFYF+V1x4lIWv?= =?us-ascii?Q?5+oiG4oAInIre6aC/XYA/NRHBnOD36r7vbBfRMcNBLAh5gDyyZkjR9rhvSfG?= =?us-ascii?Q?LTRIx5dyHu6gkahnyMOQM8oGgzVhQBJtGy6r6RdJhIuOGgwbcOPrJxWxc6s5?= =?us-ascii?Q?IZhT+TAks4kixZ0gUuLgfzsRcGDcAwAjPRieJHcSCVwU1w1DfT9FP+3aMJzo?= =?us-ascii?Q?NVv3CWWx90c5U8shUVhD4ddpHg6wKoBmaXWX4wQeRFo77xxKRfsTEdvI0CRo?= =?us-ascii?Q?r+vQ4WJnGPu1POXuZdyjJR04S/+huSmbiJqESl46rWd/+XIMH0kSNTT/i/Nx?= =?us-ascii?Q?S88QTJUDXW6HhJR0E6gw/ZRLXR9uT3W4nrn/D6esKfeD8vhT+vIGZgNTctwX?= =?us-ascii?Q?WLas74uD/ogwvlNl2XsQJJmvhuRTJjkn/ht0a2BQtP33lrRrQ6ibXDgLb+mu?= =?us-ascii?Q?WYVoqK2qcxA3TKy3iVHYpF6b+KlpspI/VZQWcFUKqkU1Q6vkIr8jOHJqaYVy?= =?us-ascii?Q?hjCq142SX7l8jQvrvQt6WUorckbcnFdtAsWpgSLOFi1jZo3zEOQPKQI7s5zX?= =?us-ascii?Q?2+a9suZavSnStGHibdCQm6A8vt9QmENx6TfvC/w8c8zEVofd3HVf0oxqz0KI?= =?us-ascii?Q?JIYS7JPTpkhmbN4V/PKrjv/VNiAoW3re7f7hmURhPJJo/PNCLmTgTCfwAM0e?= =?us-ascii?Q?KLdPcZ1RTL073IPJHyh2c8LhHi7N4lwNF3If/VDBF/i51pRPS2ElI4KQy+zc?= =?us-ascii?Q?56MrUSep0WsKJb3SB0L2r9wdaOtT3JNRVJRkhzTFv2K+A4p3VQK03wYpSMwc?= =?us-ascii?Q?QrzRqqrZUiRDMDSmDSlkpSSbt64jyGSaJ/KVxEWXqvB4MbAu9JPCVbbC8m94?= =?us-ascii?Q?bpg31KcyEmBV0Ai3q119Ssm9AQZRYaalHHcCgrKN100lJ5OIsPycC17QbNfD?= =?us-ascii?Q?UmoAQ/oHTt468uS6x3AqhIuivZsIIjauYkSnJE+8sBKj55H403GJaFStbRGr?= =?us-ascii?Q?f6nqy8r7NcyaBJqPStB7B50yl46meQaA5DJEgfj7RSd8JUukBXK6uGtfaC/C?= =?us-ascii?Q?1urJxgD8k4W/m1hTDK0CqIeeEik3BynuEDzZ/YwUnz0Yn456Z3X1e3fbcQeJ?= =?us-ascii?Q?FtSGKh0Ljyfd9EhK97T3UqzL4cAhpKZxuq6wjpgxb4KCBQTAwg4S0ejNC56c?= =?us-ascii?Q?DIlBm8bMNmc=3D?= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255;CTRY:;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:VI0PR08MB11200.eurprd08.prod.outlook.com;PTR:;CAT:NONE;SFS:(13230040)(376014)(366016)(1800799024);DIR:OUT;SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB9PR08MB9443 X-EOPAttributedMessage: 0 X-MS-Exchange-Transport-CrossTenantHeadersStripped: AM4PEPF00025F9A.EURPRD83.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: d182ba21-5766-4932-4aa8-08ddd5cf3b62 X-Microsoft-Antispam: BCL:0;ARA:13230040|14060799003|82310400026|1800799024|35042699022|36860700013|376014; X-Microsoft-Antispam-Message-Info: =?us-ascii?Q?1/wWBMLAqn8Zkvk0c5KAABPDLtdLY630+BA4D+KmLKALqkblnTMzP3yBjlM+?= =?us-ascii?Q?J+38NGt0G3ebItiq3g2p1DuDHt6UdMr50+jRLAdYycmLsRn8TdDRB5IFMS3r?= =?us-ascii?Q?1zzpY2T+xtppcxLpuvJvcylCy1STu7N2V7Ck2o0mZOdu15JuZzoDCIpHZBkp?= =?us-ascii?Q?8GVwfa9KP0YPvZx+6zw633yt6onqK/e245F1iryLYbW4Ux2nFDhzKznkMnhz?= =?us-ascii?Q?rFuX6vvjdH7SO4nFV126U+FXFXzr6ew6GBLnGcQpbUbWkzeK0RzTeDG7nN0U?= =?us-ascii?Q?NotR5Hck4dGSyN+AUAUcwsinW0LicWvtZfsUBkR+YEL1Y3DnrCZcnbBHLKug?= =?us-ascii?Q?uSM+xp+2s/82rtC+tMN63wX7nvDoajsDVTty8UnPT0wpxYryp2i8+OiQ78Z6?= =?us-ascii?Q?rpsU93yLAy4eLMcdmJbVJSa7oZB41k1cerwAiYP4UVac4ZDF9Fq4os+5qodH?= =?us-ascii?Q?BvCPMBKMQmK779ki3wZUtTl4Gnx7QkKwq+B34AzddNF19p1ClX8kQqe40ZY+?= =?us-ascii?Q?YIpi4usQPcMTBlD7StZSlUtxMSw2fu3CldBiAI9yzUEEM72LBzJ6ahmdgEu8?= =?us-ascii?Q?SJgyV064IIYYFl3dVCAAIqQwPbOEDzXFpMYC034CZ6IgDQk0s7Hq4GTDp7bV?= =?us-ascii?Q?4MlPpRyR17KonL9bm81bgU0q0ugkeyQRGsB9PfDiMTkKKvmVGbtfHtieFo2v?= =?us-ascii?Q?Tm9htgFpQxSPTck25yQs9SXyfIF+CnFWWB359gOk1lm0cpI4O3AMCo/YBNsW?= =?us-ascii?Q?bhZl3HLuZgU9yPFf35iD89fgoqd5rzbQ8XGzinpWEwTfCZStVUHpnUHoPwYX?= =?us-ascii?Q?dxgBljuI5kMR8u77l0iEeGiUrx1JiC9ZaRZSAi4aIXb+qRmTrEoxwz5sKLuv?= =?us-ascii?Q?KoAPqDAIU5ZIXLw5ThrPOHpWcm4foLnk538aQnOtt2qzPHJyWGQURgdlGKXG?= =?us-ascii?Q?ki7l8uPLtikf4O/6t8zS/QdiV7pmg485Iu3QszgePJHv4jd8zV2rBs50KYde?= =?us-ascii?Q?iu0RwStFaA0XZ9ITuf7GYIfCnfBmpXd5RX/p8+tirkttw+B286oJY8VbC1rs?= =?us-ascii?Q?ccW0AIWkQCUP6hdDHYOP/SQ8pyNODIoRyj2t0XtIBrkLyveMgpQIyUT4+K7d?= =?us-ascii?Q?etRjRlwr7a/PQqVh6xFbQSKf61qpTfd5v8Ct2+qFZV7nMJZqH52N8zC5Spum?= =?us-ascii?Q?i/hA+iR7KCKx4bPAhbRkUWXB7gkAC4X9BsssWcWwtzZ3qPwpWJAznmeh/d9u?= =?us-ascii?Q?1YE29fEh9q0o1Hdx4wfg2PJelJ2Gfn5JgBG/7AsR7awlfhDYRNDQzpj+OhNS?= =?us-ascii?Q?tPRrXPNcT1fpyYsY/7IGokQsEhvvKF0cK9v0bL1BWiTQcTXAx1LbQs14k+FM?= =?us-ascii?Q?dOceXmmjxINP3SjhGijxt8koB0LHo+N3MRhMNhf86akshXDTH8eV5rNO1jBn?= =?us-ascii?Q?LMlFmb515aLp9KmnIn9XtErY0o7ykPl65cWCv9kHUp9LVMLzf00gotbYAgtt?= =?us-ascii?Q?qki6ZHv4V5gS2GA2iDKNxe6Xljpp+XvQsDtt?= X-Forefront-Antispam-Report: CIP:4.158.2.129;CTRY:GB;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:outbound-uk1.az.dlp.m.darktrace.com;PTR:InfoDomainNonexistent;CAT:NONE;SFS:(13230040)(14060799003)(82310400026)(1800799024)(35042699022)(36860700013)(376014);DIR:OUT;SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 07 Aug 2025 16:27:30.9211 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: e7018b97-c139-4add-beb0-08ddd5cf4e9a X-MS-Exchange-CrossTenant-Id: f34e5979-57d9-4aaa-ad4d-b122a662184d X-MS-Exchange-CrossTenant-OriginalAttributedTenantConnectingIp: TenantId=f34e5979-57d9-4aaa-ad4d-b122a662184d;Ip=[4.158.2.129];Helo=[outbound-uk1.az.dlp.m.darktrace.com] X-MS-Exchange-CrossTenant-AuthSource: AM4PEPF00025F9A.EURPRD83.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB6056 Content-Type: text/plain; charset="utf-8" This patch introduces panthor_hw and moves the initialization of the gpu_info struct into panthor_hw.c in preparation of handling future GPU register and naming changes. Future GPU support can be added by extending panthor_gpu_info_init() with the necessary register reads behind GPU architecture version guards if the change is minor. For more complex changes, the function can be forked and the appropriate function will need to be called based on the GPU architecture version. Reviewed-by: Steven Price Reviewed-by: Chia-I Wu Reviewed-by: Liviu Dudau Signed-off-by: Karunika Choo --- drivers/gpu/drm/panthor/Makefile | 1 + drivers/gpu/drm/panthor/panthor_device.c | 5 + drivers/gpu/drm/panthor/panthor_gpu.c | 95 ------------------- drivers/gpu/drm/panthor/panthor_hw.c | 113 +++++++++++++++++++++++ drivers/gpu/drm/panthor/panthor_hw.h | 11 +++ 5 files changed, 130 insertions(+), 95 deletions(-) create mode 100644 drivers/gpu/drm/panthor/panthor_hw.c create mode 100644 drivers/gpu/drm/panthor/panthor_hw.h diff --git a/drivers/gpu/drm/panthor/Makefile b/drivers/gpu/drm/panthor/Mak= efile index 15294719b09c..02db21748c12 100644 --- a/drivers/gpu/drm/panthor/Makefile +++ b/drivers/gpu/drm/panthor/Makefile @@ -8,6 +8,7 @@ panthor-y :=3D \ panthor_gem.o \ panthor_gpu.o \ panthor_heap.o \ + panthor_hw.o \ panthor_mmu.o \ panthor_sched.o =20 diff --git a/drivers/gpu/drm/panthor/panthor_device.c b/drivers/gpu/drm/pan= thor/panthor_device.c index f0b2da5b2b96..81df49880bd8 100644 --- a/drivers/gpu/drm/panthor/panthor_device.c +++ b/drivers/gpu/drm/panthor/panthor_device.c @@ -18,6 +18,7 @@ #include "panthor_device.h" #include "panthor_fw.h" #include "panthor_gpu.h" +#include "panthor_hw.h" #include "panthor_mmu.h" #include "panthor_regs.h" #include "panthor_sched.h" @@ -244,6 +245,10 @@ int panthor_device_init(struct panthor_device *ptdev) return ret; } =20 + ret =3D panthor_hw_init(ptdev); + if (ret) + goto err_rpm_put; + ret =3D panthor_gpu_init(ptdev); if (ret) goto err_rpm_put; diff --git a/drivers/gpu/drm/panthor/panthor_gpu.c b/drivers/gpu/drm/pantho= r/panthor_gpu.c index cb7a335e07d7..5e2c3173ae27 100644 --- a/drivers/gpu/drm/panthor/panthor_gpu.c +++ b/drivers/gpu/drm/panthor/panthor_gpu.c @@ -37,40 +37,6 @@ struct panthor_gpu { wait_queue_head_t reqs_acked; }; =20 -/** - * struct panthor_model - GPU model description - */ -struct panthor_model { - /** @name: Model name. */ - const char *name; - - /** @arch_major: Major version number of architecture. */ - u8 arch_major; - - /** @product_major: Major version number of product. */ - u8 product_major; -}; - -/** - * GPU_MODEL() - Define a GPU model. A GPU product can be uniquely identif= ied - * by a combination of the major architecture version and the major product - * version. - * @_name: Name for the GPU model. - * @_arch_major: Architecture major. - * @_product_major: Product major. - */ -#define GPU_MODEL(_name, _arch_major, _product_major) \ -{\ - .name =3D __stringify(_name), \ - .arch_major =3D _arch_major, \ - .product_major =3D _product_major, \ -} - -static const struct panthor_model gpu_models[] =3D { - GPU_MODEL(g610, 10, 7), - {}, -}; - #define GPU_INTERRUPTS_MASK \ (GPU_IRQ_FAULT | \ GPU_IRQ_PROTM_FAULT | \ @@ -83,66 +49,6 @@ static void panthor_gpu_coherency_set(struct panthor_dev= ice *ptdev) ptdev->coherent ? GPU_COHERENCY_PROT_BIT(ACE_LITE) : GPU_COHERENCY_NONE); } =20 -static void panthor_gpu_init_info(struct panthor_device *ptdev) -{ - const struct panthor_model *model; - u32 arch_major, product_major; - u32 major, minor, status; - unsigned int i; - - ptdev->gpu_info.gpu_id =3D gpu_read(ptdev, GPU_ID); - ptdev->gpu_info.csf_id =3D gpu_read(ptdev, GPU_CSF_ID); - ptdev->gpu_info.gpu_rev =3D gpu_read(ptdev, GPU_REVID); - ptdev->gpu_info.core_features =3D gpu_read(ptdev, GPU_CORE_FEATURES); - ptdev->gpu_info.l2_features =3D gpu_read(ptdev, GPU_L2_FEATURES); - ptdev->gpu_info.tiler_features =3D gpu_read(ptdev, GPU_TILER_FEATURES); - ptdev->gpu_info.mem_features =3D gpu_read(ptdev, GPU_MEM_FEATURES); - ptdev->gpu_info.mmu_features =3D gpu_read(ptdev, GPU_MMU_FEATURES); - ptdev->gpu_info.thread_features =3D gpu_read(ptdev, GPU_THREAD_FEATURES); - ptdev->gpu_info.max_threads =3D gpu_read(ptdev, GPU_THREAD_MAX_THREADS); - ptdev->gpu_info.thread_max_workgroup_size =3D gpu_read(ptdev, GPU_THREAD_= MAX_WORKGROUP_SIZE); - ptdev->gpu_info.thread_max_barrier_size =3D gpu_read(ptdev, GPU_THREAD_MA= X_BARRIER_SIZE); - ptdev->gpu_info.coherency_features =3D gpu_read(ptdev, GPU_COHERENCY_FEAT= URES); - for (i =3D 0; i < 4; i++) - ptdev->gpu_info.texture_features[i] =3D gpu_read(ptdev, GPU_TEXTURE_FEAT= URES(i)); - - ptdev->gpu_info.as_present =3D gpu_read(ptdev, GPU_AS_PRESENT); - - ptdev->gpu_info.shader_present =3D gpu_read64(ptdev, GPU_SHADER_PRESENT); - ptdev->gpu_info.tiler_present =3D gpu_read64(ptdev, GPU_TILER_PRESENT); - ptdev->gpu_info.l2_present =3D gpu_read64(ptdev, GPU_L2_PRESENT); - - arch_major =3D GPU_ARCH_MAJOR(ptdev->gpu_info.gpu_id); - product_major =3D GPU_PROD_MAJOR(ptdev->gpu_info.gpu_id); - major =3D GPU_VER_MAJOR(ptdev->gpu_info.gpu_id); - minor =3D GPU_VER_MINOR(ptdev->gpu_info.gpu_id); - status =3D GPU_VER_STATUS(ptdev->gpu_info.gpu_id); - - for (model =3D gpu_models; model->name; model++) { - if (model->arch_major =3D=3D arch_major && - model->product_major =3D=3D product_major) - break; - } - - drm_info(&ptdev->base, - "mali-%s id 0x%x major 0x%x minor 0x%x status 0x%x", - model->name ?: "unknown", ptdev->gpu_info.gpu_id >> 16, - major, minor, status); - - drm_info(&ptdev->base, - "Features: L2:%#x Tiler:%#x Mem:%#x MMU:%#x AS:%#x", - ptdev->gpu_info.l2_features, - ptdev->gpu_info.tiler_features, - ptdev->gpu_info.mem_features, - ptdev->gpu_info.mmu_features, - ptdev->gpu_info.as_present); - - drm_info(&ptdev->base, - "shader_present=3D0x%0llx l2_present=3D0x%0llx tiler_present=3D0x%0llx", - ptdev->gpu_info.shader_present, ptdev->gpu_info.l2_present, - ptdev->gpu_info.tiler_present); -} - static void panthor_gpu_irq_handler(struct panthor_device *ptdev, u32 stat= us) { gpu_write(ptdev, GPU_INT_CLEAR, status); @@ -205,7 +111,6 @@ int panthor_gpu_init(struct panthor_device *ptdev) spin_lock_init(&gpu->reqs_lock); init_waitqueue_head(&gpu->reqs_acked); ptdev->gpu =3D gpu; - panthor_gpu_init_info(ptdev); =20 dma_set_max_seg_size(ptdev->base.dev, UINT_MAX); pa_bits =3D GPU_MMU_FEATURES_PA_BITS(ptdev->gpu_info.mmu_features); diff --git a/drivers/gpu/drm/panthor/panthor_hw.c b/drivers/gpu/drm/panthor= /panthor_hw.c new file mode 100644 index 000000000000..94f170a8e5c5 --- /dev/null +++ b/drivers/gpu/drm/panthor/panthor_hw.c @@ -0,0 +1,113 @@ +// SPDX-License-Identifier: GPL-2.0 or MIT +/* Copyright 2025 ARM Limited. All rights reserved. */ + +#include "panthor_device.h" +#include "panthor_hw.h" +#include "panthor_regs.h" + +/** + * struct panthor_model - GPU model description + */ +struct panthor_model { + /** @name: Model name. */ + const char *name; + + /** @arch_major: Major version number of architecture. */ + u8 arch_major; + + /** @product_major: Major version number of product. */ + u8 product_major; +}; + +/** + * GPU_MODEL() - Define a GPU model. A GPU product can be uniquely identif= ied + * by a combination of the major architecture version and the major product + * version. + * @_name: Name for the GPU model. + * @_arch_major: Architecture major. + * @_product_major: Product major. + */ +#define GPU_MODEL(_name, _arch_major, _product_major) \ +{\ + .name =3D __stringify(_name), \ + .arch_major =3D _arch_major, \ + .product_major =3D _product_major, \ +} + +static const struct panthor_model gpu_models[] =3D { + GPU_MODEL(g610, 10, 7), + {}, +}; + +static void panthor_gpu_info_init(struct panthor_device *ptdev) +{ + unsigned int i; + + ptdev->gpu_info.gpu_id =3D gpu_read(ptdev, GPU_ID); + ptdev->gpu_info.csf_id =3D gpu_read(ptdev, GPU_CSF_ID); + ptdev->gpu_info.gpu_rev =3D gpu_read(ptdev, GPU_REVID); + ptdev->gpu_info.core_features =3D gpu_read(ptdev, GPU_CORE_FEATURES); + ptdev->gpu_info.l2_features =3D gpu_read(ptdev, GPU_L2_FEATURES); + ptdev->gpu_info.tiler_features =3D gpu_read(ptdev, GPU_TILER_FEATURES); + ptdev->gpu_info.mem_features =3D gpu_read(ptdev, GPU_MEM_FEATURES); + ptdev->gpu_info.mmu_features =3D gpu_read(ptdev, GPU_MMU_FEATURES); + ptdev->gpu_info.thread_features =3D gpu_read(ptdev, GPU_THREAD_FEATURES); + ptdev->gpu_info.max_threads =3D gpu_read(ptdev, GPU_THREAD_MAX_THREADS); + ptdev->gpu_info.thread_max_workgroup_size =3D gpu_read(ptdev, GPU_THREAD_= MAX_WORKGROUP_SIZE); + ptdev->gpu_info.thread_max_barrier_size =3D gpu_read(ptdev, GPU_THREAD_MA= X_BARRIER_SIZE); + ptdev->gpu_info.coherency_features =3D gpu_read(ptdev, GPU_COHERENCY_FEAT= URES); + for (i =3D 0; i < 4; i++) + ptdev->gpu_info.texture_features[i] =3D gpu_read(ptdev, GPU_TEXTURE_FEAT= URES(i)); + + ptdev->gpu_info.as_present =3D gpu_read(ptdev, GPU_AS_PRESENT); + + ptdev->gpu_info.shader_present =3D gpu_read64(ptdev, GPU_SHADER_PRESENT); + ptdev->gpu_info.tiler_present =3D gpu_read64(ptdev, GPU_TILER_PRESENT); + ptdev->gpu_info.l2_present =3D gpu_read64(ptdev, GPU_L2_PRESENT); +} + +static void panthor_hw_info_init(struct panthor_device *ptdev) +{ + const struct panthor_model *model; + u32 arch_major, product_major; + u32 major, minor, status; + + panthor_gpu_info_init(ptdev); + + arch_major =3D GPU_ARCH_MAJOR(ptdev->gpu_info.gpu_id); + product_major =3D GPU_PROD_MAJOR(ptdev->gpu_info.gpu_id); + major =3D GPU_VER_MAJOR(ptdev->gpu_info.gpu_id); + minor =3D GPU_VER_MINOR(ptdev->gpu_info.gpu_id); + status =3D GPU_VER_STATUS(ptdev->gpu_info.gpu_id); + + for (model =3D gpu_models; model->name; model++) { + if (model->arch_major =3D=3D arch_major && + model->product_major =3D=3D product_major) + break; + } + + drm_info(&ptdev->base, + "mali-%s id 0x%x major 0x%x minor 0x%x status 0x%x", + model->name ?: "unknown", ptdev->gpu_info.gpu_id >> 16, + major, minor, status); + + drm_info(&ptdev->base, + "Features: L2:%#x Tiler:%#x Mem:%#x MMU:%#x AS:%#x", + ptdev->gpu_info.l2_features, + ptdev->gpu_info.tiler_features, + ptdev->gpu_info.mem_features, + ptdev->gpu_info.mmu_features, + ptdev->gpu_info.as_present); + + drm_info(&ptdev->base, + "shader_present=3D0x%0llx l2_present=3D0x%0llx tiler_present=3D0x%0llx", + ptdev->gpu_info.shader_present, ptdev->gpu_info.l2_present, + ptdev->gpu_info.tiler_present); +} + +int panthor_hw_init(struct panthor_device *ptdev) +{ + panthor_hw_info_init(ptdev); + + return 0; +} diff --git a/drivers/gpu/drm/panthor/panthor_hw.h b/drivers/gpu/drm/panthor= /panthor_hw.h new file mode 100644 index 000000000000..0af6acc6aa6a --- /dev/null +++ b/drivers/gpu/drm/panthor/panthor_hw.h @@ -0,0 +1,11 @@ +/* SPDX-License-Identifier: GPL-2.0 or MIT */ +/* Copyright 2025 ARM Limited. All rights reserved. */ + +#ifndef __PANTHOR_HW_H__ +#define __PANTHOR_HW_H__ + +struct panthor_device; + +int panthor_hw_init(struct panthor_device *ptdev); + +#endif /* __PANTHOR_HW_H__ */ --=20 2.49.0 From nobody Sun Oct 5 05:29:01 2025 Received: from AM0PR02CU008.outbound.protection.outlook.com (mail-westeuropeazon11013047.outbound.protection.outlook.com [52.101.72.47]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id 16E4226F45D for ; Thu, 7 Aug 2025 16:27:43 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=fail smtp.client-ip=52.101.72.47 ARC-Seal: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584067; cv=fail; b=A8OB+FL3vQBIkdhhyXtJhFgxdTgE2j7+JtLEer3onPFoNe793BEZj0EqJ8DHpdJe7cwqqZzvhfvUH+bDEEE/u6BbyS0ObO2p37K0tZZvZfwPvc253ywpElH0mv+bjXPu+3qxbhhj3enJV7G6lMatyhEshE1aPeylfuG0g8sGyGI= ARC-Message-Signature: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584067; c=relaxed/simple; bh=9euFAuP6N2eWKaHlRQ8f4tsAHvY1/8YTobFMDWqnIFo=; h=From:To:Cc:Subject:Date:Message-ID:In-Reply-To:References: Content-Type:MIME-Version; b=iyJe6HtGa7K2hMuBEBzcfdMPRaFAD+THuLnu5Bb3K8qihWpi96xWTzi7Aggfo/Bi5O1P2hIpuxpdbgTJaK5cE+6mb0obR6OPoLpBpHb8SsCnlzzHUd1mtZfz5gkoF5fnpS6+ik/FG3pb/r7wyYLce92l0H/NUz7OlsyvW43YNT0= ARC-Authentication-Results: i=3; smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com; spf=pass smtp.mailfrom=arm.com; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=aBjrmVA5; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=aBjrmVA5; arc=fail smtp.client-ip=52.101.72.47 Authentication-Results: smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com Authentication-Results: smtp.subspace.kernel.org; spf=pass smtp.mailfrom=arm.com Authentication-Results: smtp.subspace.kernel.org; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="aBjrmVA5"; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="aBjrmVA5" ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=TgjQ0vEI/jy0zx/JlDd0Fx8FvYGb9TEKrx1LFu5oVG1WrifiTaBxTQ3mn+B6unrZHTymg5G7vFenNJt9TfPYSfqG/reqJmte1cGCAf9Z4ZWgsTAHB4O2nMxfhXO1EjJq+S9RF0c+Vr/EKXxMQ6jYYm6N3EhXrOzgyk5lmCyJnnUcGr1zOipJRebgUC9dWEp/I7MhJeCPVLeqBsbbADOyTih0EwChpnLtbNEGufDSyOV2z73ZPMtSf+KpawvK0bqv8HQN4tFrXqZeVzoSHvHkGeNkOpXZ5+rdX7ILStfswR9MhvyR2u6d4e3qfpbucFjTquk//VfQ4x4+j30+QAapZw== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=olrCtt/Jc/BYZMAJJcGgK7N2XyUhPzjhKdJH/GOKCuo=; b=ul8BLjvvvp3J1dcyOYswxOF0R8/EyGQp3X89okYci5fDDqC3fjPp8wz5eBGcGMquhg9hLt+9NJqbV5/wEp8P90xZM+QTWSnEOggxmAgSPBcDfO2stM39JZ/wA35ainyTr+Z3XU32deuWpO8JKub5nS9pvO6Cy6ir3/RbU3tmW8yw6gLybZMFfymBxVPlkYWnX1lEP+NHtms/nBxuAiVGqAft7k65Z1+Je8oO2sUJJUwhKl3nlwdWPSaCT0Gt1cCqb/2RyZF+Z2aXC7J405CPMl5lLYgWBCjiJU+dGw/pw4O5Lon5EkdIRAyxo33CSPlKexdP5R4JOldAg0L/FgDE2w== ARC-Authentication-Results: i=2; mx.microsoft.com 1; spf=pass (sender ip is 4.158.2.129) smtp.rcpttodomain=lists.freedesktop.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=pass (signature was verified) header.d=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=olrCtt/Jc/BYZMAJJcGgK7N2XyUhPzjhKdJH/GOKCuo=; b=aBjrmVA5AdIZVEa6q31XxA5yts33BHu+4uEiy0fe9CE9qd5mO3zKQ66ZyxCdX5Lb+QK2IEWaydJC95+r6PZzGaYsTzQzD1UGbF9TL1GkZnorC7ca3Pacj3ktnZ+2NWTSSYnVfh+SCH2RLGVuay8haMrOHxk5S6uHhee7hgd87hg= Received: from CWLP265CA0380.GBRP265.PROD.OUTLOOK.COM (2603:10a6:401:5e::32) by AS2PR08MB8477.eurprd08.prod.outlook.com (2603:10a6:20b:55b::15) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.8989.20; Thu, 7 Aug 2025 16:27:36 +0000 Received: from AM4PEPF00027A5E.eurprd04.prod.outlook.com (2603:10a6:401:5e:cafe::8a) by CWLP265CA0380.outlook.office365.com (2603:10a6:401:5e::32) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.16 via Frontend Transport; Thu, 7 Aug 2025 16:27:36 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 4.158.2.129) smtp.mailfrom=arm.com; dkim=pass (signature was verified) header.d=arm.com;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 4.158.2.129 as permitted sender) receiver=protection.outlook.com; client-ip=4.158.2.129; helo=outbound-uk1.az.dlp.m.darktrace.com; pr=C Received: from outbound-uk1.az.dlp.m.darktrace.com (4.158.2.129) by AM4PEPF00027A5E.mail.protection.outlook.com (10.167.16.72) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.8 via Frontend Transport; Thu, 7 Aug 2025 16:27:36 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=taM8veIbUNOD6FWXpcirHMSWCF85pbTJqBWbF3nGYqSZHF0mCSRE2O3MxhUeT0I0TL53Gomg8y/PW1OV133q19TJBkJN6zh6aTg4onplBr0CJpdhfURV9hmDH8WVn2KWhM1Rt0TVpKdTbcv5Vp1rHBzyzzIesNLlq1JB5jIqk4dYvFvQqG5flGXIYplVjTWylOs56gNuIgay7DIgL8pLS5MF4WtoU12b2R5WMdJUh5hsDgmTau/4bIlSyxBNuppF9YKCyH3Ro1CJiYz/dprPCYSgeCE5uXvKqmi62o+Wm+sx1mVoOzCSwGZ4rfZc8rSE6na6kipuDBnPClfj4cAKIg== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=olrCtt/Jc/BYZMAJJcGgK7N2XyUhPzjhKdJH/GOKCuo=; b=lA7fEPidSX9SlzkbJlOIsqmUb2zt9lrhw1B6+kvu1HZdhLJ5aSx30tdOkUe+nPZ3VoSPBNxbT6vbdOvDr/DW9TlBuJJLtJfySTl/tYGwfSSydqGdfpYSzSxs1PR4Crx9snHjO0V2uF6zyPrkGOPeYtU4xY7XmkPyPc4xM15mVf40yzxt4UPjVakNfSxQgIKT246oy6DYQNtnz/Mq/7V9wQvejIj6UMbzRQ3foyG+uLpuhZ87xmKQ5VhgBGGyzykoj0XD3+vtAT7iWLU5wGBzuEOb67vKLzw8/bkGWhLdVSjK0VUwTRS5hnc43Yk2Mp6a+ecHfcFCL55ibKOYIN4txw== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=olrCtt/Jc/BYZMAJJcGgK7N2XyUhPzjhKdJH/GOKCuo=; b=aBjrmVA5AdIZVEa6q31XxA5yts33BHu+4uEiy0fe9CE9qd5mO3zKQ66ZyxCdX5Lb+QK2IEWaydJC95+r6PZzGaYsTzQzD1UGbF9TL1GkZnorC7ca3Pacj3ktnZ+2NWTSSYnVfh+SCH2RLGVuay8haMrOHxk5S6uHhee7hgd87hg= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) by DB9PR08MB9443.eurprd08.prod.outlook.com (2603:10a6:10:45b::19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.13; Thu, 7 Aug 2025 16:27:04 +0000 Received: from VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74]) by VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74%5]) with mapi id 15.20.9009.016; Thu, 7 Aug 2025 16:27:04 +0000 From: Karunika Choo To: dri-devel@lists.freedesktop.org Cc: nd@arm.com, Boris Brezillon , Steven Price , Liviu Dudau , Maarten Lankhorst , Maxime Ripard , Thomas Zimmermann , David Airlie , Simona Vetter , linux-kernel@vger.kernel.org, Chia-I Wu Subject: [PATCH v9 2/7] drm/panthor: Simplify getting the GPU model name Date: Thu, 7 Aug 2025 17:26:28 +0100 Message-ID: <20250807162633.3666310-3-karunika.choo@arm.com> X-Mailer: git-send-email 2.49.0 In-Reply-To: <20250807162633.3666310-1-karunika.choo@arm.com> References: <20250807162633.3666310-1-karunika.choo@arm.com> Content-Transfer-Encoding: quoted-printable X-ClientProxiedBy: LO2P265CA0450.GBRP265.PROD.OUTLOOK.COM (2603:10a6:600:e::30) To VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) Precedence: bulk X-Mailing-List: linux-kernel@vger.kernel.org List-Id: List-Subscribe: List-Unsubscribe: MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: VI0PR08MB11200:EE_|DB9PR08MB9443:EE_|AM4PEPF00027A5E:EE_|AS2PR08MB8477:EE_ X-MS-Office365-Filtering-Correlation-Id: d6f0a6a9-d215-4e46-3e8e-08ddd5cf51ac X-LD-Processed: f34e5979-57d9-4aaa-ad4d-b122a662184d,ExtAddr,ExtAddr x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|376014|366016|1800799024; X-Microsoft-Antispam-Message-Info-Original: =?us-ascii?Q?20CIN0IZdbHbt0lvqI6XOeuzAPWcVNYyiR7oDn5y+FhYDri6ELj5i3Zs/uYf?= =?us-ascii?Q?rLd2LZ+ujmkX0hsR7YEqo2cP91Dp9PIV2rj2eT3me59NcC+fioiXDHFUwzjb?= =?us-ascii?Q?h6/F1yNamlTb7OSH+xCR8V+/vt86nczvis47TFJTzi0cupcOncXwhDPXZQ7O?= =?us-ascii?Q?IP5Qn1TUhdtcTvjN3ffWKZtjbzNeGhFIWW+wsLt5/jQqfXr58ZaW+9TedDxV?= =?us-ascii?Q?1U4KzJJO6dT5mCYZHjZTOILAL/2XEBlrSkl8+ykbeavaJFFv7/LA0JmjwcAU?= =?us-ascii?Q?RT0EPbKVs0sIzM1QnISy92TvL88PdiOho6eBj2u2Awys/WZ9AyE+VXix/zv1?= =?us-ascii?Q?gn8d2fURE3kS7oROXW29Ep2m/xWd7VgleTLW0kMIdeUJxujXpLMuXQiUAU2W?= =?us-ascii?Q?S1bJVxSZOrZ/aFFMCkcFqtwp+x5sVpW7x2RAsql/AabGMRhkH9E0hG2Dq/mI?= =?us-ascii?Q?swLi1tngcNA+rO17p/FQI7du1FVxmfQ/dAr0UIZRjFvgEEElcdDlxuaOE4BK?= =?us-ascii?Q?q0Axf1yQH0/cOswI3nqPYRXEjE/7IiQQe2z4FOY9zNUYrdiWVr6q/9BLx9/b?= =?us-ascii?Q?soubnovc77ZKmqm5vfF4f0Y6XkLzsppi2v0suaZ/9PHZy4jPL9oh2DnckDQO?= =?us-ascii?Q?W2ax1UyRjRF8XSJI8INexiyexVcB3XdoMLrMTT1tOnBtEbNsTFYvy2JEmaJq?= =?us-ascii?Q?DGg6zY+4TtJde2GfQFrJWX10rQEPyf+Mjcv2A467aLcVuaKJZuhAUhj61q+i?= =?us-ascii?Q?oBsl2x3eTcmPc/VDXHuCVF2nVASo65M3KtZm2ntnSP4JUFJFaHhehgxG+oN8?= =?us-ascii?Q?ZzRmlXFEAC191UDwTkgKW4/7pIFhOnWwDcpO6JvM5SurFPgvvrH2hdMi+33E?= =?us-ascii?Q?5ZoUnbyjYt4GWzzp6Up7XnBp4cThg8XADd7pklenTtwwlLBfO3rQ/re2jcq7?= =?us-ascii?Q?zqQc1ztmdUXCs8wLCr6h1CBNvcxKrytmNuIaE/VGnP5KwjjMWJ4MZJQbblV7?= =?us-ascii?Q?R1jBDMZkQ388TbXwQN/4qQQwvSEkmdLHPUss6U/6Y35TDqSF5gUYuXNUt2S0?= =?us-ascii?Q?3qrvQKXpmvj6etmVnotB/1s4Qt4k5E7/j85rkAVTM4P74XrRvd7y3YS7KK24?= =?us-ascii?Q?+Xqy2QmK1lrR4Dnq86hDN04Vkt53SOTpF5EVfOiLTTz4CYfl+PAICeGWCaAR?= =?us-ascii?Q?UAbVAWwUMKwJr7lPMyvwlg/3dAl8i0tHmSDaiKQH1SFxKD/JST1lf/xY24Pm?= =?us-ascii?Q?UG2kKZ7+EmDTCFqd36zQ5aFJNyVxJMMqJvzMyiQGKADSUKA/Jk+fPoX8wqdg?= =?us-ascii?Q?VX2tLFPkOkP+CaF0Q8HVVCx+jT+R5y/vstYlFI2lKmy0IVTH4Kct6poy5fQ6?= =?us-ascii?Q?qd92CU49DFKNQipqC5g2mTolC1bwE/beXNuc4CMPOaVBS4OZvCJKmwJS4Q65?= =?us-ascii?Q?889yO/oabRg=3D?= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255;CTRY:;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:VI0PR08MB11200.eurprd08.prod.outlook.com;PTR:;CAT:NONE;SFS:(13230040)(376014)(366016)(1800799024);DIR:OUT;SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB9PR08MB9443 X-EOPAttributedMessage: 0 X-MS-Exchange-Transport-CrossTenantHeadersStripped: AM4PEPF00027A5E.eurprd04.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 5aeba8ba-ed2c-45f4-fcfc-08ddd5cf3e7e X-Microsoft-Antispam: BCL:0;ARA:13230040|376014|35042699022|14060799003|36860700013|1800799024|82310400026; X-Microsoft-Antispam-Message-Info: =?us-ascii?Q?UIftNhUzpgwJSijGN1Wcgv+rxUB78Uitgkv/k1po1KNLgdjo/R+bF30utgRR?= =?us-ascii?Q?tiWzyVeMHdTvaNg8nQDOomgBakSE3f02AqiaAncZqD3qDBwNPxQHd/8mLe4H?= =?us-ascii?Q?HNFOfQ6qXdd9LjUQuO1kic/yUB1zb6B6T/w9WffLg16PdaNnEppAMcOjHMLg?= =?us-ascii?Q?+d1X+MTSSnlrCJfgbgy3U5XtCkInaVY3uOhd1q8JtJeQShsuGMk1Svhxz+hA?= =?us-ascii?Q?3uoqGdmgg5EGsZDPrrU3SVWTuBCfqhXWtfxaweDKfserejnB7rAlCsBGC8R8?= =?us-ascii?Q?OWWyZA6qBbwv13xj8VBMhq4cWvjiZu7na3h44SMMc7wmjbo2ks+xz/0ly3j6?= =?us-ascii?Q?UVDXe2TX6s+Il/O82agJ6k3Y/FyJf0lMv0FD3e6kTbWI4GwAOthMWqGbIrH7?= =?us-ascii?Q?G8J2wZEQTLb2WR1F2MI3dDq/33SLErlDEmO2QvEi54kxPtIE8BfDNZZ4chPj?= =?us-ascii?Q?xQDUL9AqXgBxKXo2HVvPflSURKtQk4FzsZxaq0+B54AvsgMskqKdGTvMpxdT?= =?us-ascii?Q?m22FbFyqQ+S63Jm+PdY6olQXvrvlNL9qaA80hCULs50nrIRmaWdFV+3ngIZ/?= =?us-ascii?Q?BaKT07MjrhzCyCItCbEZuj8Yi8EKBmHVJKtbaFi6VHJsYqdK9rJWhIlfojg9?= =?us-ascii?Q?GEoohnWSEUIUfmybX1zTb2NnY741AsPNMCvDBAbq9ibUzSMl3sgQpB6vGAvj?= =?us-ascii?Q?lBy4wTQkC15leIbcKpgYZQXD8cS4I5FLNWKMOIaxX4KS77UdUjvUpOQ4Bhqq?= =?us-ascii?Q?WK3uln2vAwLDYtrB4J68MVTIAy2Dva7t9kU0ZNYqhoGMx0MivpBdfTOMC4MR?= =?us-ascii?Q?le0HxOzOb0yAGWVA+IIpt2JmLppJXiUYlJpAn6TjvLEkNf6Oi6eIbZq2y6Q2?= =?us-ascii?Q?nXHHAPbkEOsLYmaUnJ87bBcQET3iR2cYSCq6UQ1tscSjZ8T4ct5pjJ4ufdAS?= =?us-ascii?Q?1S87jVW7ilVm0fGsdmlzyuDR8vFwXGmPVm9eMqHZt2o0VeaoaFVOlCnaiplA?= =?us-ascii?Q?qyEVK+JvMcOVzGtuaRYMAHTFIXrjkuhC6tRpdwRkspUHhmmkgToKQyf4uiZa?= =?us-ascii?Q?VfArbadYEjS4r4N8HLziLA75Kyfwun2C3FYK/d9qlXx2jBGzoV1FkgZelOOh?= =?us-ascii?Q?jD1W+SfQ1clIpSrU7LyngW1nIb2ooL+Wn2fN97RRGB9i5lhXnUv4gBu53s4+?= =?us-ascii?Q?71ESYiT+t5DBXyV4TpxdwUpniznRZAa/B4B2e+Fvt63+oXk/g4yyXvA8Bl0T?= =?us-ascii?Q?g8u8TXYBwVdMaB5j5Y6ecdj+5nkQdSASTGLHy7Yg7DG9inTKGDT2wVkDOAgu?= =?us-ascii?Q?shj5amkxet6NO0D68GD44hrZdmSeTAAw+Y/oVdKxAJ/eWMnA2puR3wYRwu9b?= =?us-ascii?Q?ut2MguRPCXBgQ5v7JNCN1QHB0yQUokdCg+5TUZQwgLiEd3TsoM4lqxYhZ3Dq?= =?us-ascii?Q?2wpG5fllqZWbjYr+Y/gPBcTkcEh2ZBK0k6RPJ/WOgMCHXnXQjLGqJveg9qy2?= =?us-ascii?Q?Dsy62CZLc3YUwx7P/tKH23yuskYMHwzI1j68?= X-Forefront-Antispam-Report: CIP:4.158.2.129;CTRY:GB;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:outbound-uk1.az.dlp.m.darktrace.com;PTR:InfoDomainNonexistent;CAT:NONE;SFS:(13230040)(376014)(35042699022)(14060799003)(36860700013)(1800799024)(82310400026);DIR:OUT;SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 07 Aug 2025 16:27:36.0736 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: d6f0a6a9-d215-4e46-3e8e-08ddd5cf51ac X-MS-Exchange-CrossTenant-Id: f34e5979-57d9-4aaa-ad4d-b122a662184d X-MS-Exchange-CrossTenant-OriginalAttributedTenantConnectingIp: TenantId=f34e5979-57d9-4aaa-ad4d-b122a662184d;Ip=[4.158.2.129];Helo=[outbound-uk1.az.dlp.m.darktrace.com] X-MS-Exchange-CrossTenant-AuthSource: AM4PEPF00027A5E.eurprd04.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS2PR08MB8477 Content-Type: text/plain; charset="utf-8" This patch replaces the panthor_model structure with a simple switch case based on the product_id which is in the format of: ((arch_major << 24) | product_major) This simplifies comparison and allows extending of the function to accommodate naming differences based on supported GPU features. Reviewed-by: Steven Price Reviewed-by: Chia-I Wu Reviewed-by: Liviu Dudau Signed-off-by: Karunika Choo --- drivers/gpu/drm/panthor/panthor_hw.c | 61 ++++++++-------------------- 1 file changed, 17 insertions(+), 44 deletions(-) diff --git a/drivers/gpu/drm/panthor/panthor_hw.c b/drivers/gpu/drm/panthor= /panthor_hw.c index 94f170a8e5c5..6bff69fd247e 100644 --- a/drivers/gpu/drm/panthor/panthor_hw.c +++ b/drivers/gpu/drm/panthor/panthor_hw.c @@ -5,39 +5,22 @@ #include "panthor_hw.h" #include "panthor_regs.h" =20 -/** - * struct panthor_model - GPU model description - */ -struct panthor_model { - /** @name: Model name. */ - const char *name; - - /** @arch_major: Major version number of architecture. */ - u8 arch_major; - - /** @product_major: Major version number of product. */ - u8 product_major; -}; - -/** - * GPU_MODEL() - Define a GPU model. A GPU product can be uniquely identif= ied - * by a combination of the major architecture version and the major product - * version. - * @_name: Name for the GPU model. - * @_arch_major: Architecture major. - * @_product_major: Product major. - */ -#define GPU_MODEL(_name, _arch_major, _product_major) \ -{\ - .name =3D __stringify(_name), \ - .arch_major =3D _arch_major, \ - .product_major =3D _product_major, \ -} +#define GPU_PROD_ID_MAKE(arch_major, prod_major) \ + (((arch_major) << 24) | (prod_major)) + +static char *get_gpu_model_name(struct panthor_device *ptdev) +{ + const u32 gpu_id =3D ptdev->gpu_info.gpu_id; + const u32 product_id =3D GPU_PROD_ID_MAKE(GPU_ARCH_MAJOR(gpu_id), + GPU_PROD_MAJOR(gpu_id)); + + switch (product_id) { + case GPU_PROD_ID_MAKE(10, 7): + return "Mali-G610"; + } =20 -static const struct panthor_model gpu_models[] =3D { - GPU_MODEL(g610, 10, 7), - {}, -}; + return "(Unknown Mali GPU)"; +} =20 static void panthor_gpu_info_init(struct panthor_device *ptdev) { @@ -68,27 +51,17 @@ static void panthor_gpu_info_init(struct panthor_device= *ptdev) =20 static void panthor_hw_info_init(struct panthor_device *ptdev) { - const struct panthor_model *model; - u32 arch_major, product_major; u32 major, minor, status; =20 panthor_gpu_info_init(ptdev); =20 - arch_major =3D GPU_ARCH_MAJOR(ptdev->gpu_info.gpu_id); - product_major =3D GPU_PROD_MAJOR(ptdev->gpu_info.gpu_id); major =3D GPU_VER_MAJOR(ptdev->gpu_info.gpu_id); minor =3D GPU_VER_MINOR(ptdev->gpu_info.gpu_id); status =3D GPU_VER_STATUS(ptdev->gpu_info.gpu_id); =20 - for (model =3D gpu_models; model->name; model++) { - if (model->arch_major =3D=3D arch_major && - model->product_major =3D=3D product_major) - break; - } - drm_info(&ptdev->base, - "mali-%s id 0x%x major 0x%x minor 0x%x status 0x%x", - model->name ?: "unknown", ptdev->gpu_info.gpu_id >> 16, + "%s id 0x%x major 0x%x minor 0x%x status 0x%x", + get_gpu_model_name(ptdev), ptdev->gpu_info.gpu_id >> 16, major, minor, status); =20 drm_info(&ptdev->base, --=20 2.49.0 From nobody Sun Oct 5 05:29:01 2025 Received: from PA4PR04CU001.outbound.protection.outlook.com (mail-francecentralazon11013003.outbound.protection.outlook.com [40.107.162.3]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id BC78226FA6A for ; Thu, 7 Aug 2025 16:27:46 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=fail smtp.client-ip=40.107.162.3 ARC-Seal: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584069; cv=fail; b=ZCqVZiJhewBxAUUMhEz5uKPgEkFqDu0tTPtkx1Nu1rW2BCZHz7w8M/0JPv7t2gkFoZCRiUneiqq6j5Y043JC52dNoNDYMR0b2vMLPCH9RBONzIZknNSp37kocBYhYXYW1E4p44WzfKX4/oDxXjrpuB9ooBlsKqclr695YuOrwgM= ARC-Message-Signature: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584069; c=relaxed/simple; bh=hn5vI93y7iY2Ytwt8rOYtLiupWOysUXrPlgXJtuLrCg=; h=From:To:Cc:Subject:Date:Message-ID:In-Reply-To:References: Content-Type:MIME-Version; b=I9MxjUpD/vgrUqqWrVb9XRvT4/OnEeEe0yKQOJNZjam8Q6Am6RE2zeiygbQFnrNGIlpXCMlL4h/jvZQYX4R+WMKys/hixg652J39iopfQbzErvZ+zpC8R5TUF3HyiqkncObxajUizxoNCTxXhrS8MVtBS66FvF4TsJuZeAxFONo= ARC-Authentication-Results: i=3; smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com; spf=pass smtp.mailfrom=arm.com; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=IbLRBEPx; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=IbLRBEPx; arc=fail smtp.client-ip=40.107.162.3 Authentication-Results: smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com Authentication-Results: smtp.subspace.kernel.org; spf=pass smtp.mailfrom=arm.com Authentication-Results: smtp.subspace.kernel.org; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="IbLRBEPx"; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="IbLRBEPx" ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=Eh2UlSd3wK60qW33Iz5n6IJuq9RxymNkfLnRA18HBJ1VCwTKshrRHGVHDfhL+m9+SyHjvmfOWwICdeJbRuWgbIaz5Lf8r1r0DWKB4dZvqS70Xww/jj0hw/FEnAdbYLQ6WefZ6F4zjP5VKb2LdVbo+Czhhmt1OATK8CQvxu2ZRVDKa1QgxlT4ELfhmUUdAZACJ+fz8Cqy9fJ3IC4cD5HokWSr7k0QzxjG21V18xmmLTKpTSAx2spwRAXzmdImg8UjEiPVYYNI8at1EvKXwX5fQvvN1/MoDOyGmQpaZS1aGnIsrzeFIdbyYhtkMLO1vHJOzWOcslvxYMxwT38qHY2AXA== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=jnSbabYdty3yAXpc4tkZIDjTYpp8vcumtAW5e9NFEhY=; b=Lxa1OaGi+ezjxi6aoY4p3EYSYBYelXeZ5zzNM7n+9R0wsve64gwCvB3V6jUjtWVanc8VuNY4wXWxvQldpwmW1s6YMaL5DpNCdQkCZ7zZLGlSqJY0a6rPYuZJ57tvgVOt9Od3gUpreY5CaBiHPa5jb/dF5ff6F+HE6ml1mRQlpCwZpjBZQk2exP1vXSQCDkVMVhKt+nzVkcFkcD+INajVxXcCaSMu+pwfh8WwMUDwsLMXm38g6/6dzyu3IOm5naHKDvF/vZqve8WltV3UsyNot9tSKlK8enCG6+S2ykRS9m6UyRAel3otTjemVttC1Ybs6Uy9q6XKPV9sMx85k9SGSw== ARC-Authentication-Results: i=2; mx.microsoft.com 1; spf=pass (sender ip is 4.158.2.129) smtp.rcpttodomain=lists.freedesktop.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=pass (signature was verified) header.d=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=jnSbabYdty3yAXpc4tkZIDjTYpp8vcumtAW5e9NFEhY=; b=IbLRBEPx5itmNKee4Lhbp7NsgLn51NB2VyFI9I0eDHtYxPu11pqUOkjyMo1jAn8IUDVyFFwRemAfy/DSbMwCJrZ9p6aslnQV1+3/pgy7gUQHb08PwC5SZ2kTvslFCF3KelIh+DGHNFIwX3alK/fGu0C1R6fohFVy3OU6OWD91P4= Received: from AS4PR09CA0011.eurprd09.prod.outlook.com (2603:10a6:20b:5e0::13) by AS8PR08MB6551.eurprd08.prod.outlook.com (2603:10a6:20b:319::13) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.14; Thu, 7 Aug 2025 16:27:41 +0000 Received: from AM4PEPF00027A60.eurprd04.prod.outlook.com (2603:10a6:20b:5e0:cafe::f7) by AS4PR09CA0011.outlook.office365.com (2603:10a6:20b:5e0::13) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.16 via Frontend Transport; Thu, 7 Aug 2025 16:27:41 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 4.158.2.129) smtp.mailfrom=arm.com; dkim=pass (signature was verified) header.d=arm.com;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 4.158.2.129 as permitted sender) receiver=protection.outlook.com; client-ip=4.158.2.129; helo=outbound-uk1.az.dlp.m.darktrace.com; pr=C Received: from outbound-uk1.az.dlp.m.darktrace.com (4.158.2.129) by AM4PEPF00027A60.mail.protection.outlook.com (10.167.16.68) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.8 via Frontend Transport; Thu, 7 Aug 2025 16:27:41 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=w4zhye5TfgYrECQO6ESTxOF9/wScLseujBqn0pB7hbpYTWWx0n+MRvFqegutmwbBxy+DQx9z9tDKmSkggz7ELuP0qYyZBN8jL7PcTM6T0OVimMmD9AJeKiscEmp9/aueUutb8yGP8956/2F6xRmNPxvq3Hew79SnpqJvW4AwvX5xyctc45ukgpwFcTPyIIgJOc++qObK7pQ9KDne4hh1Yeus42HpN7MA69frfWdJPHeGsA5IS3n7/YhCbNskFoF9JcWzfjg+o/Sm9mp6n1SE9cOWVFJTeSUQwM7aEhnbSU0TDqVvgtOirJ4RtcYUKr3MDdQ4skD5TORQzWtlrT+2nA== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=jnSbabYdty3yAXpc4tkZIDjTYpp8vcumtAW5e9NFEhY=; b=rLbS5F/IjY+EE3URNJLExw2l6L3OvUCVORuhH9a8LE8bcPgNmM+ALF3h+FhRwD9pQn80uv07Cd/NWT8s9Keky3qUL0oy/FZ4Me0WAeTzqq0Jpk9S9VlkTWo5/35u8w0GNAH7YapeeV50Vw/puaxULhTyWRLlQbq2ZVirPwUT3iWLSwkF5kp3LgGL1J0Pe0iSm8jr0z9cMRufWHL62mMXstNjMCLjcofsrQlcMtNzqX0N/bxE6Gr4pKwYKRACQa4wdQrx0WNlndMvZl/zj3ePao+iLPs3iVbvsmvt7Hym25zJqgn8ebArVbUfntyF/y4C4Nr2bBtpjatGGXTPVTgewQ== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=jnSbabYdty3yAXpc4tkZIDjTYpp8vcumtAW5e9NFEhY=; b=IbLRBEPx5itmNKee4Lhbp7NsgLn51NB2VyFI9I0eDHtYxPu11pqUOkjyMo1jAn8IUDVyFFwRemAfy/DSbMwCJrZ9p6aslnQV1+3/pgy7gUQHb08PwC5SZ2kTvslFCF3KelIh+DGHNFIwX3alK/fGu0C1R6fohFVy3OU6OWD91P4= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) by DB9PR08MB9443.eurprd08.prod.outlook.com (2603:10a6:10:45b::19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.13; Thu, 7 Aug 2025 16:27:08 +0000 Received: from VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74]) by VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74%5]) with mapi id 15.20.9009.016; Thu, 7 Aug 2025 16:27:07 +0000 From: Karunika Choo To: dri-devel@lists.freedesktop.org Cc: nd@arm.com, Boris Brezillon , Steven Price , Liviu Dudau , Maarten Lankhorst , Maxime Ripard , Thomas Zimmermann , David Airlie , Simona Vetter , linux-kernel@vger.kernel.org, Chia-I Wu Subject: [PATCH v9 3/7] drm/panthor: Add support for Mali-G710, Mali-G510 and Mali-G310 Date: Thu, 7 Aug 2025 17:26:29 +0100 Message-ID: <20250807162633.3666310-4-karunika.choo@arm.com> X-Mailer: git-send-email 2.49.0 In-Reply-To: <20250807162633.3666310-1-karunika.choo@arm.com> References: <20250807162633.3666310-1-karunika.choo@arm.com> Content-Transfer-Encoding: quoted-printable X-ClientProxiedBy: LO4P265CA0131.GBRP265.PROD.OUTLOOK.COM (2603:10a6:600:2c6::12) To VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) Precedence: bulk X-Mailing-List: linux-kernel@vger.kernel.org List-Id: List-Subscribe: List-Unsubscribe: MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: VI0PR08MB11200:EE_|DB9PR08MB9443:EE_|AM4PEPF00027A60:EE_|AS8PR08MB6551:EE_ X-MS-Office365-Filtering-Correlation-Id: 02a8b98d-acef-4c30-420b-08ddd5cf54a7 X-LD-Processed: f34e5979-57d9-4aaa-ad4d-b122a662184d,ExtAddr,ExtAddr x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|376014|366016|1800799024; X-Microsoft-Antispam-Message-Info-Original: =?us-ascii?Q?l6Gb8KtRJj2T1MVSXSMBjLBMleiYleKoMu8ikEx2cZbvo8nBF8hg0MFkXLSr?= =?us-ascii?Q?dSv1s7c2H9+8kmIHpd8zBFP+79Zhe1HGsWWLywoWonjmu0ZuDEKlRWov4gGa?= =?us-ascii?Q?OM9P7HfxFcXqsjJnaGqAdi8Z8xG3IEBVwpKrMwMo4L6d5DP5sZ55vNWHEGWB?= =?us-ascii?Q?Q8Qsn7fnB+aJPmndwIj2OX7SsrTGoe6Wau7+dtZQOr8Y5nMqNHHDvBvCAVkn?= =?us-ascii?Q?NQtatllgLEfNvlgalaJdV4V6Md20NwG807aTKuu2jwfTDZmQFu4nlB3uVzyC?= =?us-ascii?Q?+4iCrJaiC3Bwd69ykoNonDhxlwInRu94RO2ZI5Q5lQZwD4FSnRsEcCJLK1K9?= =?us-ascii?Q?tIN0sspaVTTiCejBHQV5ssfMf3VSMLYh9x69+i8oCb1DH6sOGfaw0r2ppTPH?= =?us-ascii?Q?svivcdZjS1ulbj08/gYXk/oDQYJynM9Y1+OTNMiJZsiJau4SFf0LZDvGVtmQ?= =?us-ascii?Q?GiSm3/p3zKN+790tj9HoJfMPEQb8fOuNdavYDv5ZdmzYj6/tYvNEZ8PR+zcM?= =?us-ascii?Q?wsva1VPl7ZhUOygnDykXP2ziwf+cHKooAuSGyioCOArPxSeyShTub1kCowxf?= =?us-ascii?Q?GBPFjQZXWEQEO8hNaVOkhFU4JQGFYZv6Es2TB8xGDGQ0NcWhv0eGckSIVE1m?= =?us-ascii?Q?Gw868xpjf5YIPMe+jpLdeHWcpXNS+D7lADHLgCxpF2Rc7fYYNUxXSeT/WKVp?= =?us-ascii?Q?Td7cnEVmHL8lE/32+sKzSnwPlk0fCH00RMzY1Gjm6nWr4ec5jeG4Qrm/uHBj?= =?us-ascii?Q?5TClgQForFLkFOuV0Uj3ChtQv8VQBRmWeU2xHN8VnM8UKxWk/YSSCEWZciq9?= =?us-ascii?Q?bW2Omj4OdBH+P7zfMpRo6ira1GOYpwAwZzNpgOc4xjRFgJHQzXymcLX/PIpD?= =?us-ascii?Q?VZpRXF6iiEl4eE9sAFo4j2q6v4q35WTpBzwLh6XoLMOH3fXg6tHuJoF+XBmO?= =?us-ascii?Q?fB0Z7h6Hn6QaB2Qg88uLYuXaoHLUum9bnVTpPXo1s+0ngvXPKx+oKRPz3RQI?= =?us-ascii?Q?VWosd4EuHz/vQOVMNnD6q2IUbSTCWYMhS0UC4rx38B1qRzJ89k6cofWmNpHs?= =?us-ascii?Q?SYPVQWRdWoSUJI6D4Id46a+bQn3PxEhfLvDTSGddlJBWynstUp2kB4KUwQMN?= =?us-ascii?Q?IahT7pqXGztXSREVqdbD8besScHfpGks1OVgOqy+5HpqcHQPK3WE9Qrw0KlK?= =?us-ascii?Q?ia9XRJzCCcbVFJmvUPLjqA7AyfTBNo3vcY2dfg9vIeGdPrZ+zSyzs4s4iS8W?= =?us-ascii?Q?Aen742KE5/A7K/o4OMLuHaNfQIzYG81PKJM6ouKVtEKvPhjnO48DIE4sxyEy?= =?us-ascii?Q?EvfpPwwc6OgrsxUW031aNKZe8iRbXHBfD9DZFlsywDaDFVnAOIjBmAy/XEv8?= =?us-ascii?Q?Tc3m7IMx2/tBpzRvsqVkOt2q0n2z/TIJTViDyKlRMn0ExTBtZw=3D=3D?= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255;CTRY:;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:VI0PR08MB11200.eurprd08.prod.outlook.com;PTR:;CAT:NONE;SFS:(13230040)(376014)(366016)(1800799024);DIR:OUT;SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB9PR08MB9443 X-EOPAttributedMessage: 0 X-MS-Exchange-Transport-CrossTenantHeadersStripped: AM4PEPF00027A60.eurprd04.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: af2b0c6c-197e-4869-9bc6-08ddd5cf4095 X-Microsoft-Antispam: BCL:0;ARA:13230040|82310400026|35042699022|14060799003|1800799024|36860700013|376014; X-Microsoft-Antispam-Message-Info: =?us-ascii?Q?SO4xLJfo78hiZ1/75bjdafzHxAq0lM+0WK9vESSWTBDu6vQG0l/0xgG2D9qD?= =?us-ascii?Q?UkJboi4UyRr8vsmOXfsr27m3VacLLiYUHcByoef2nOin40l3jVxSeTcKa5YC?= =?us-ascii?Q?hN5ZNgPZD1IDSGSowyOaiKHhMcf5wO3coH7dyqkeLidPHZlsMIfJAhA60dsi?= =?us-ascii?Q?p5ETFWgdRU/R90P7mSdgDAT+AEp2aqxJqr3hZNkCsOeZQo818XjWUnfL9Roi?= =?us-ascii?Q?1y/ZwWG6wVPY1JtsDUFeYqYUT/QNmeSqhoFNPVnHNF31t305sBaS42iFUHUe?= =?us-ascii?Q?44D05oZ/zrFVChJ7c3JDaevM5T4guwrMQfSQUnLZg2/emcYwNEn64vq1o6k8?= =?us-ascii?Q?I+p7K7NsdPS4Pgk724EvW3eHQ3q574REIn7c74oel7OdyJCZIFJR6NYGg/Uz?= =?us-ascii?Q?Ormzs4z79btzPpdxlR0fEo3zBbs8yWmjfezSd5cXvktf5WPpI7g3JS+0B3eZ?= =?us-ascii?Q?D5+SEAr8h57tfdYxSVGqpe1JqpVEv1gEJpfEerG2f7UqoPavdTluf5SOZapY?= =?us-ascii?Q?JK7O/SBkukOaoQAmS1kS3K9CdtLEhmJjRr9zkFXe7bEf7bkAFdqIkPGglgAt?= =?us-ascii?Q?Btw5wyhx6b1+iSYcnVFCrJgnGaOed8kqeW9vYQLm9agpuXCfjJEl9G+qQrDi?= =?us-ascii?Q?iJk+irD50HVl8p7ndFc4cOgKpBnxUwftq2eoJmESJ3/KGrVo4KFftOGCy75w?= =?us-ascii?Q?fVKV3TorQLQMFx1jgATJ+C1rGgmtmXpt04Ns+hP3qDBqzZ47iLH+dMsxkMvs?= =?us-ascii?Q?8KGjXD+oNKPJsZBDSbNfRWyULRxc7bl44dxIL2zw8eonBNr5Pa+uhneIxXtQ?= =?us-ascii?Q?DUCDd0ObNkiHMJ29Tg/baBjn1UTmHYlIkYglliP6nDkMMqELbcvpmYHh/VwW?= =?us-ascii?Q?O5Ohr+//WIjPxPXe4vS/4UHEwbcXV5tRHyCrlPI+QLPQkJOgZXNDwmUSWRX5?= =?us-ascii?Q?vI4Uz7FoRV2TsQsxivVVbAdEQQIUlJ4CxuTwCZDtkSt8XeD/Q67S1ZtESXai?= =?us-ascii?Q?4CLtX/sqicCewzUBNdpMzzhyAt51/wNvBdBgSEj/6kuZdIUgDBxcBQ3KK1p9?= =?us-ascii?Q?lKb8RvrV1zfnOWcTr5NBdr8j8ZeC8Xyf7f35zESK3PVyTYL5j/h9Cd90Pdah?= =?us-ascii?Q?MUbBvd1o7G6j86x/sTwTww9tj2ZLRn2YdYtdYbDG1SuWNCCcW+tf5sbBO9KO?= =?us-ascii?Q?Yv+W7K1WYPDUnBS7xz7wm+FykzWQyeELoDETsUpFDl206GUe7OzztIdVgOP7?= =?us-ascii?Q?ceu47g7WopXIHTJeiFJyNRN57nFOE2BM5SEfky38Q3ELS2PWcdNBO8cZD+pX?= =?us-ascii?Q?u3lsTnxsDy3g8e9wcDtvQpEVQGAELrYSGlf7aiGkgWi7dVPItyKVh4CuVvBQ?= =?us-ascii?Q?k+W7Qt/d2fA6N2aIHOe+jkXxrJLMjt20R+5rREDZ73ovalWTCvpLDcTXXq7U?= =?us-ascii?Q?OYe+IzzETKP2va2lFB8XoShBIHlbhzJflcfJRXStgbOu+0driqy4uFQcCs4l?= =?us-ascii?Q?emP37T9QrN0m/gw+n9LULhmy6dI3P3t6K9cc?= X-Forefront-Antispam-Report: CIP:4.158.2.129;CTRY:GB;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:outbound-uk1.az.dlp.m.darktrace.com;PTR:InfoDomainNonexistent;CAT:NONE;SFS:(13230040)(82310400026)(35042699022)(14060799003)(1800799024)(36860700013)(376014);DIR:OUT;SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 07 Aug 2025 16:27:41.0681 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 02a8b98d-acef-4c30-420b-08ddd5cf54a7 X-MS-Exchange-CrossTenant-Id: f34e5979-57d9-4aaa-ad4d-b122a662184d X-MS-Exchange-CrossTenant-OriginalAttributedTenantConnectingIp: TenantId=f34e5979-57d9-4aaa-ad4d-b122a662184d;Ip=[4.158.2.129];Helo=[outbound-uk1.az.dlp.m.darktrace.com] X-MS-Exchange-CrossTenant-AuthSource: AM4PEPF00027A60.eurprd04.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB6551 Content-Type: text/plain; charset="utf-8" This patch adds GPU model name and FW binary support for Mali-G710, Mali-G510, and Mali-G310. Reviewed-by: Steven Price Reviewed-by: Chia-I Wu Reviewed-by: Liviu Dudau Signed-off-by: Karunika Choo --- drivers/gpu/drm/panthor/panthor_fw.c | 2 ++ drivers/gpu/drm/panthor/panthor_hw.c | 6 ++++++ 2 files changed, 8 insertions(+) diff --git a/drivers/gpu/drm/panthor/panthor_fw.c b/drivers/gpu/drm/panthor= /panthor_fw.c index 36f1034839c2..b7b454d16f12 100644 --- a/drivers/gpu/drm/panthor/panthor_fw.c +++ b/drivers/gpu/drm/panthor/panthor_fw.c @@ -1402,3 +1402,5 @@ int panthor_fw_init(struct panthor_device *ptdev) } =20 MODULE_FIRMWARE("arm/mali/arch10.8/mali_csffw.bin"); +MODULE_FIRMWARE("arm/mali/arch10.10/mali_csffw.bin"); +MODULE_FIRMWARE("arm/mali/arch10.12/mali_csffw.bin"); diff --git a/drivers/gpu/drm/panthor/panthor_hw.c b/drivers/gpu/drm/panthor= /panthor_hw.c index 6bff69fd247e..6d2ad3c8cb5e 100644 --- a/drivers/gpu/drm/panthor/panthor_hw.c +++ b/drivers/gpu/drm/panthor/panthor_hw.c @@ -15,6 +15,12 @@ static char *get_gpu_model_name(struct panthor_device *p= tdev) GPU_PROD_MAJOR(gpu_id)); =20 switch (product_id) { + case GPU_PROD_ID_MAKE(10, 2): + return "Mali-G710"; + case GPU_PROD_ID_MAKE(10, 3): + return "Mali-G510"; + case GPU_PROD_ID_MAKE(10, 4): + return "Mali-G310"; case GPU_PROD_ID_MAKE(10, 7): return "Mali-G610"; } --=20 2.49.0 From nobody Sun Oct 5 05:29:01 2025 Received: from AM0PR02CU008.outbound.protection.outlook.com (mail-westeuropeazon11013032.outbound.protection.outlook.com [52.101.72.32]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id 4DC7226FDA4 for ; Thu, 7 Aug 2025 16:27:53 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=fail smtp.client-ip=52.101.72.32 ARC-Seal: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584076; cv=fail; b=cqsdifvKj5ApJ3o5nkxLhosac+5ZFSFOwMf3+vDNFWt6R+tMHUOQqmKeZ7t0zJEbhBmyHS6PYiPgs+UX8wxLDEtm4he8MTbrcmgsYH8QM8cmG9lgv7ZbRc1pwsYxpJcR9qadB3FLZ/DN46WXE3rZCKn4mKoaMp50w4+10GFM2Zk= ARC-Message-Signature: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584076; c=relaxed/simple; bh=ee5zsy1V3AOVmtf7a2Wpp7RK7qHmnewvhfuA7drC7FE=; h=From:To:Cc:Subject:Date:Message-ID:In-Reply-To:References: Content-Type:MIME-Version; b=dqUaXspIf8ZgDBZUFZ7EFPLKXGBpwTtnLMqp8FLrLEvBf18VzDGWXXWgvVdfeTNXiLV/qs/jvsE3QWuRFex14DqXczpBOcCBJSfNjKMYj6mkbV6Bg7S0+1OiNkcIn9ci2sVKIKryRQNVvoqAADH6abfzEQqCUmh1xOuI03+SaUc= ARC-Authentication-Results: i=3; smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com; spf=pass smtp.mailfrom=arm.com; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=aB6LsiUR; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=aB6LsiUR; arc=fail smtp.client-ip=52.101.72.32 Authentication-Results: smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com Authentication-Results: smtp.subspace.kernel.org; spf=pass smtp.mailfrom=arm.com Authentication-Results: smtp.subspace.kernel.org; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="aB6LsiUR"; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="aB6LsiUR" ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=D7NBsRWD8d+I0/464ama93vy+oKzWUUZ4/7+yM4ewwHIrErNfe5o5p90VdUwkdAANI7+zX4gJKcmp410K61jS7O11ftSB7Kp3/LxfmuVdCAB7KRvurDuKo4clb4MxDJjtmk02oG5yjZLFDXN/nqTY1fb1rumoWazoh2FNvI7jDOqb8eSpI+tqJkqozeEoBFZD+TLNlVVOI+eGUwyxLRqSqys+uU4uMDJz7GJHHAdSdnI5QbN4mcdQSdZang9kroSl4lU/Ef3gAiyxoTml/HUwpsgTy9FFsPFC/zzLpLLa702dXqifPxVxl+lofp8r0oXlkpcQSl+HYJcj8K+zS9fPQ== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=3mjgVoDuFVFbCu37TmdReHBn3HfnSCYbKodLzFSwml8=; b=SZV8lxFvb9dHqeoHMdBzBbI6WHkrxD2ktDqElQdkJq6RAy6jOGTXOHYZOt+4hH3utLOs5HTDn/wxBmBcU5aRvTdWH/r3TIv2wsm9Ar7y6pR/KU6YbEE7lnY60I2DRu6EOJTCKqjwV1M6I3HBMM/uNDRYYvryErvqeEQCyRYp1sdzUrnEb9xuPgyJ/OnfuuOg+D8AFjgatjD0Gs+xhWPnJA8nWHlI3w8+bibvfzyiti9sbv5ysd+TsfijKRSwmccDl27Xob6OiiIelqYvAtwqyIpH0krgb5JSLbN1wOTLT/PiJVfAQfw7U6IP/5IUROBo3J4x9hus12Cnoj17Yrpj8w== ARC-Authentication-Results: i=2; mx.microsoft.com 1; spf=pass (sender ip is 4.158.2.129) smtp.rcpttodomain=lists.freedesktop.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=pass (signature was verified) header.d=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=3mjgVoDuFVFbCu37TmdReHBn3HfnSCYbKodLzFSwml8=; b=aB6LsiURKGue8hCCxmDkhAZSmY7bWDJglXHiKB2s52BHEoysv5NwP86NCINUw3EgOtaJacKwS1iW2am2YdXN3Mxn9z4s1jBtt1XIWUuVZpi9R1HeE5V/iFaYMmSh9ElXLF0AbieC5LYJo2mZx/JXgkYoY8Dm4qtQfVd5OQxer6k= Received: from CWLP123CA0144.GBRP123.PROD.OUTLOOK.COM (2603:10a6:401:87::36) by GVXPR08MB11058.eurprd08.prod.outlook.com (2603:10a6:150:1f6::22) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.14; Thu, 7 Aug 2025 16:27:44 +0000 Received: from AMS1EPF00000048.eurprd04.prod.outlook.com (2603:10a6:401:87:cafe::b) by CWLP123CA0144.outlook.office365.com (2603:10a6:401:87::36) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.8989.21 via Frontend Transport; Thu, 7 Aug 2025 16:27:44 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 4.158.2.129) smtp.mailfrom=arm.com; dkim=pass (signature was verified) header.d=arm.com;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 4.158.2.129 as permitted sender) receiver=protection.outlook.com; client-ip=4.158.2.129; helo=outbound-uk1.az.dlp.m.darktrace.com; pr=C Received: from outbound-uk1.az.dlp.m.darktrace.com (4.158.2.129) by AMS1EPF00000048.mail.protection.outlook.com (10.167.16.132) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.8 via Frontend Transport; Thu, 7 Aug 2025 16:27:43 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=kWUYJiUvdQSNxmdxQFdpKuR//EWEJrTgIMyMHgF+Qepow2XQ86gmRELBrIVgm1W7irjNeSWTmuAUshrAOV8xtAv9ZZWw/p+YW5OvJY0tNfaB7+YXtaM0SwTeDUBhcrLVqbuKHTNry96ntrieDxPKM1FAHTFkrkHJ9teHMTXuRqtj/IETX68cIQRaX9JA52w3IhchEa82ei3Cpj7EdAFHiOQiH1sptLnTi+fCfnB0iMwxYRCzUrwtWuFL2Wul0fvk6cGX1yyS19er3xKxgxA+9n8F+re/lg++EKrGVKfahlBavwazdQbJVFzWtO6hxF+OVjtHkJMvCqnrNtVfDULVbg== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=3mjgVoDuFVFbCu37TmdReHBn3HfnSCYbKodLzFSwml8=; b=kgnBXo2Y/3BlAv9qzttJwfLMv2wlZT0f4kOCYcixGMBiboU8MyNw+GR+7tpIMZ6lkoeo2Ah0o/P6Jd6Uo6n+glyLh4x8kx3dFHKnSjmu/tODHkfbXEJquAGpegh7vbOK7nMJgaKKu9dPbyRyD79q07eRcF/cHw7z3K4cW5Jc3RgBaZnePJq30w/WnTZpqqyMNe3xbHnHyRfN+tozPN0V99HlYUNgiQe1UdJC67qJ7GdDKEtXzFU5wp14u/VE6Ghs/F7SIing0KhFAU83PMBK1Hu/+njpJ/ql+pZe9jsSsejnXVYR47QQ8bb2RXAnL90L3TF214K10tB0V2/7lwmUeA== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=3mjgVoDuFVFbCu37TmdReHBn3HfnSCYbKodLzFSwml8=; b=aB6LsiURKGue8hCCxmDkhAZSmY7bWDJglXHiKB2s52BHEoysv5NwP86NCINUw3EgOtaJacKwS1iW2am2YdXN3Mxn9z4s1jBtt1XIWUuVZpi9R1HeE5V/iFaYMmSh9ElXLF0AbieC5LYJo2mZx/JXgkYoY8Dm4qtQfVd5OQxer6k= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) by DB9PR08MB9443.eurprd08.prod.outlook.com (2603:10a6:10:45b::19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.13; Thu, 7 Aug 2025 16:27:11 +0000 Received: from VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74]) by VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74%5]) with mapi id 15.20.9009.016; Thu, 7 Aug 2025 16:27:11 +0000 From: Karunika Choo To: dri-devel@lists.freedesktop.org Cc: nd@arm.com, Boris Brezillon , Steven Price , Liviu Dudau , Maarten Lankhorst , Maxime Ripard , Thomas Zimmermann , David Airlie , Simona Vetter , linux-kernel@vger.kernel.org, Chia-I Wu Subject: [PATCH v9 4/7] drm/panthor: Add support for Mali-Gx15 family of GPUs Date: Thu, 7 Aug 2025 17:26:30 +0100 Message-ID: <20250807162633.3666310-5-karunika.choo@arm.com> X-Mailer: git-send-email 2.49.0 In-Reply-To: <20250807162633.3666310-1-karunika.choo@arm.com> References: <20250807162633.3666310-1-karunika.choo@arm.com> Content-Transfer-Encoding: quoted-printable X-ClientProxiedBy: LO4P123CA0244.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:1a7::15) To VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) Precedence: bulk X-Mailing-List: linux-kernel@vger.kernel.org List-Id: List-Subscribe: List-Unsubscribe: MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: VI0PR08MB11200:EE_|DB9PR08MB9443:EE_|AMS1EPF00000048:EE_|GVXPR08MB11058:EE_ X-MS-Office365-Filtering-Correlation-Id: 84a478fb-33b6-40eb-e297-08ddd5cf561b X-LD-Processed: f34e5979-57d9-4aaa-ad4d-b122a662184d,ExtAddr,ExtAddr x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|376014|366016|1800799024; X-Microsoft-Antispam-Message-Info-Original: =?us-ascii?Q?HzuEr/eadLOdD//TOp0D8y+BZ4ZZSbcb42Qye1rXOLkL70YVa0/kZqRn3taW?= =?us-ascii?Q?DLh11pg+TJvx5ZNfDSJvyYCRY0bIbwRvTCZvFnBRngUbki9UDHO+mepn3NxO?= =?us-ascii?Q?W8eobpsBrQ92veh4VCe1fQUqy9Ai/uMwnJoUTWTH00p5TRsSTAsGJKqS+ftX?= =?us-ascii?Q?Af+SOYRY9c0nAbZpKxD9ieYKe31sIeJO7fq6haO9uOe3kQ/s2S20Z5fa2f4h?= =?us-ascii?Q?O4+UaNUu3Le/ew2U7vIF1tARZNaXIvd6hFZQzyImijlYBnUqCz08RSlWVP76?= =?us-ascii?Q?FGidCYTS1F3N4b0UmkEylM73AJvVhDgp8rmhfCzZxiAqyYzUlLeh+TVutpHI?= =?us-ascii?Q?Uzvs11X+j6c1TrUoPY2xX0sl+s79R0E4sbeyX9zJQoKp3a6UlYSbvAZVM3Uq?= =?us-ascii?Q?iaLH/saEgFYYZ9Gr1fagSb3VCxP4AaGTxZMwRWLHdVm3YDsELWipTOczreT/?= =?us-ascii?Q?5QPlSuIUv3mU1NPGDMnVPw44VFT9AsxK1tjixU/CE20qa9n0go20a30l+n59?= =?us-ascii?Q?hNYIG1PF/6Mf8+XN8Uw4TBNFB/2eHSWFogsxVo9ngwEVchMh+zEGk+9+Tg69?= =?us-ascii?Q?eS1NhynVuq0KxVj0mA/4jpNMr0hx4fRa0rlvryoPUJlj7j4vCGM+Cf0oFdu5?= =?us-ascii?Q?6tSxVlknUlvBepT8DQ2k5BkMdDvwyeP7n10ERTaQJbSxtqX9uzUbLikXfCAp?= =?us-ascii?Q?TZ9aG5k8wqoPWYdoLuNLiO4pf1XngyrED+pKZEKMBv1mddRx5P/PBM2pcIZA?= =?us-ascii?Q?32ET0AEZtPkAu7f1RSd1vf/kKdZuY2PtLHFf08NBRRC3yQ3ioVOJFFV9UuPF?= =?us-ascii?Q?UI1+Km92Kz/dGQ3K6/NV/ALVzBOz7ubyz9V7YJ5LZG5XG0DilTUmmenm/Et7?= =?us-ascii?Q?pYGgvaCJkiUAcHRtGRaAsFunKWPqV+RY4p84PTzLuQngMjF89cGbZuW96t3w?= =?us-ascii?Q?N7qcUgvusLBehGS5f4l9DWg/m382OT4PI5aorYbKowvMUpADHPyCRIbo/PAr?= =?us-ascii?Q?CvpYtkzfhtAT6muIhBw0aVPUzsmVgu4a/PwDDQr1YIvGatUEGdfrUJEfPDey?= =?us-ascii?Q?y6oF6tnZ62zJgsPTfx95Ku2kGJ+tzUW3emVinGQZtz2kuaWQx7xj7B/iTUeY?= =?us-ascii?Q?+b8P6HCJq3rLhxb055Z39WEAGnbertypsTUtEtewUtHIyW54RI48tjxi0Fws?= =?us-ascii?Q?eIBZpM0IIij5sT6lFCq5l1uVHAHyR4Bi7yS97SDlJ+ejKt3JyN4FhXeQ2e1B?= =?us-ascii?Q?XaQYy0kMg3rLJi/F1iwNg7r2aSEFQfJf9EqMw5JifpB5FhFC329AgLOCL2B2?= =?us-ascii?Q?+AQ/3O6Ke/s4oaqkkW4/yjI6iRRiMRaI7LDaWCw5fmEGu0ydLOQpupaAhNA0?= =?us-ascii?Q?NIND+IMTU8IXVW4YJjFdb8zvq5C3RthI9bX/11zKxrka06avDA=3D=3D?= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255;CTRY:;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:VI0PR08MB11200.eurprd08.prod.outlook.com;PTR:;CAT:NONE;SFS:(13230040)(376014)(366016)(1800799024);DIR:OUT;SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB9PR08MB9443 X-EOPAttributedMessage: 0 X-MS-Exchange-Transport-CrossTenantHeadersStripped: AMS1EPF00000048.eurprd04.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: e2d7676a-f156-4505-a18e-08ddd5cf42e5 X-Microsoft-Antispam: BCL:0;ARA:13230040|14060799003|1800799024|376014|82310400026|35042699022|36860700013; X-Microsoft-Antispam-Message-Info: =?us-ascii?Q?v4pQbi81ESM49coTvuLmMNxvkG8i+P+z4NiDRqEdNPszB9/huZ7k6galxb5X?= =?us-ascii?Q?zZNEbtXbF7DJJsb17kMA+P+7/kapvg2VazF3r+bK7VGhvKBA06uEEOafp6Tr?= =?us-ascii?Q?IgwMtouW9HPzOi+ZR2SoQo1DBW3UT3xInl/JEtzXkgg/H+8I4bTjUsPFJ04H?= =?us-ascii?Q?jszQpifPXnz87nJgqLhfbjQpR+J29Dl19n2Pqd2BRuYgOm49VLhhUzKOt7Tr?= =?us-ascii?Q?swyvykqQ2qdRwRuBIWNmq9BZyCKZR9uqcuAYKwh2mlpz1ZbKYRDS35D/Axtv?= =?us-ascii?Q?avPS/hzBK0fRU20KUvNmoQ3W8CKJqccUK4URzQiCNHlhs6L9G8RKcoKDA3q3?= =?us-ascii?Q?4LmKOJKFdEdE2qIDBdcK7+0s1nVXBBvZnD4qx3GToK+z6onqW/FOcDEdTWRR?= =?us-ascii?Q?nAD/YrUqiEZr4LIz0AVlFAEYodI2+FVHkFFrtNxJ9sKPnFgll2gU4S1mWIvR?= =?us-ascii?Q?FSRs67sB+s0JzjVPlf807EIKxjji5p2mPjkqBZcxzvi67crwo8JEfKz5NBYe?= =?us-ascii?Q?V8Tv2QX1Y3HZ2E+d1Fje0x1T0T59NwbFb+DuWCj3e6h9FMWMgU4yxacyRyBd?= =?us-ascii?Q?CyK0xC3QmL/7v8yHKGBMLZDa/tawd5/oTfOhWRcCUo53Z+A+qNUdJxS/e1uq?= =?us-ascii?Q?jqDWiXlDWkkZEkcWH0RcCirTAz8Tv7gLZfuxYS1aFDpBbjfePIoGW+mFY2Iz?= =?us-ascii?Q?Cu8Pql4Qk5gFSbfsX+7EhyOnMeSoPG2LKyjB1g6HZvfzi+etRUkCJxjkbc1a?= =?us-ascii?Q?4OgzvLHcWnmT2VjOn8nGK+En59dRKmUz2xqdK+MwYcJe1YvYPmtTCkaSX1/3?= =?us-ascii?Q?YaJcIpiDW5pax1Pti8tM1JEsdNnJEJMfVV5bXGGv4KDeJHvHF5lW5zt32C68?= =?us-ascii?Q?s2CsJqgkfAmF2MCrQ1Z+RvXQmZ1fYgyzck2aQVX1PI3kcIiTEpupZMIrfKsm?= =?us-ascii?Q?RZUpUYy0A+4KX9sG/wdRyI+7uQCuOoMOVOKGema9aFN9xzK21SDWWxDU7xTD?= =?us-ascii?Q?PqFoYEkP6jpbwlIU1eJzK3viZQUCv0dFlxCpx9+yGhao+7QL8ba/dxjhfL0D?= =?us-ascii?Q?VRbB+QyX1/JcV4IibQPiNoRElfv8d6PX7lTHEMX40sMalSE/9ACz6HiN5f2C?= =?us-ascii?Q?WpqUVbtkI87v+4POjWmrKaGgL/yd1MhYaRJpa2nVMLaRz2sKJWhMY1BdtA/R?= =?us-ascii?Q?6gU4C4DyK1TNFPsWwelmyrw5C0JEcKYtAtrfeTsohqQz0NFL36uafp/LgM/P?= =?us-ascii?Q?70lfMv1yqB/X46aSjUsUuqDSfeQgMV6xORBF5mty58cZw4Wq36FOCBFuihwy?= =?us-ascii?Q?3zG8f+AtXmlbGwnCuvD+36t3Aud5BWc3qoMuThY328Twd/R45mY6UPyS5bTR?= =?us-ascii?Q?mrzlTcuCE8EsnbjGqJJsmwiLPYSCmoiHAufMEP1vR9XQewYmARumFqVkM2kh?= =?us-ascii?Q?KBY7BynrRlEwDOPrT5VMsW3+k8tRIH+SEu5zVx1RgdnvdVXGXxeEvEAn/uPy?= =?us-ascii?Q?SW1SrFlwe4+382PPqLW5ro7xje7kZAYH9rLi?= X-Forefront-Antispam-Report: CIP:4.158.2.129;CTRY:GB;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:outbound-uk1.az.dlp.m.darktrace.com;PTR:InfoDomainNonexistent;CAT:NONE;SFS:(13230040)(14060799003)(1800799024)(376014)(82310400026)(35042699022)(36860700013);DIR:OUT;SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 07 Aug 2025 16:27:43.5232 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: 84a478fb-33b6-40eb-e297-08ddd5cf561b X-MS-Exchange-CrossTenant-Id: f34e5979-57d9-4aaa-ad4d-b122a662184d X-MS-Exchange-CrossTenant-OriginalAttributedTenantConnectingIp: TenantId=f34e5979-57d9-4aaa-ad4d-b122a662184d;Ip=[4.158.2.129];Helo=[outbound-uk1.az.dlp.m.darktrace.com] X-MS-Exchange-CrossTenant-AuthSource: AMS1EPF00000048.eurprd04.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: GVXPR08MB11058 Content-Type: text/plain; charset="utf-8" Mali-Gx15 introduces a new GPU_FEATURES register that provides information about GPU-wide supported features. The register value will be passed on to userspace via gpu_info. Additionally, Mali-Gx15 presents an 'Immortalis' naming variant depending on the shader core count and presence of Ray Intersection feature support. This patch adds: - support for correctly identifying the model names for Mali-Gx15 GPUs. - arch 11.8 FW binary support Reviewed-by: Steven Price Reviewed-by: Chia-I Wu Reviewed-by: Liviu Dudau Signed-off-by: Karunika Choo --- drivers/gpu/drm/panthor/panthor_fw.c | 1 + drivers/gpu/drm/panthor/panthor_hw.c | 15 +++++++++++++++ drivers/gpu/drm/panthor/panthor_regs.h | 3 +++ include/uapi/drm/panthor_drm.h | 3 +++ 4 files changed, 22 insertions(+) diff --git a/drivers/gpu/drm/panthor/panthor_fw.c b/drivers/gpu/drm/panthor= /panthor_fw.c index b7b454d16f12..fa6e0b48a0b2 100644 --- a/drivers/gpu/drm/panthor/panthor_fw.c +++ b/drivers/gpu/drm/panthor/panthor_fw.c @@ -1404,3 +1404,4 @@ int panthor_fw_init(struct panthor_device *ptdev) MODULE_FIRMWARE("arm/mali/arch10.8/mali_csffw.bin"); MODULE_FIRMWARE("arm/mali/arch10.10/mali_csffw.bin"); MODULE_FIRMWARE("arm/mali/arch10.12/mali_csffw.bin"); +MODULE_FIRMWARE("arm/mali/arch11.8/mali_csffw.bin"); diff --git a/drivers/gpu/drm/panthor/panthor_hw.c b/drivers/gpu/drm/panthor= /panthor_hw.c index 6d2ad3c8cb5e..8c041e1074a1 100644 --- a/drivers/gpu/drm/panthor/panthor_hw.c +++ b/drivers/gpu/drm/panthor/panthor_hw.c @@ -13,6 +13,9 @@ static char *get_gpu_model_name(struct panthor_device *pt= dev) const u32 gpu_id =3D ptdev->gpu_info.gpu_id; const u32 product_id =3D GPU_PROD_ID_MAKE(GPU_ARCH_MAJOR(gpu_id), GPU_PROD_MAJOR(gpu_id)); + const bool ray_intersection =3D !!(ptdev->gpu_info.gpu_features & + GPU_FEATURES_RAY_INTERSECTION); + const u8 shader_core_count =3D hweight64(ptdev->gpu_info.shader_present); =20 switch (product_id) { case GPU_PROD_ID_MAKE(10, 2): @@ -23,6 +26,15 @@ static char *get_gpu_model_name(struct panthor_device *p= tdev) return "Mali-G310"; case GPU_PROD_ID_MAKE(10, 7): return "Mali-G610"; + case GPU_PROD_ID_MAKE(11, 2): + if (shader_core_count > 10 && ray_intersection) + return "Mali-G715-Immortalis"; + else if (shader_core_count >=3D 7) + return "Mali-G715"; + + fallthrough; + case GPU_PROD_ID_MAKE(11, 3): + return "Mali-G615"; } =20 return "(Unknown Mali GPU)"; @@ -53,6 +65,9 @@ static void panthor_gpu_info_init(struct panthor_device *= ptdev) ptdev->gpu_info.shader_present =3D gpu_read64(ptdev, GPU_SHADER_PRESENT); ptdev->gpu_info.tiler_present =3D gpu_read64(ptdev, GPU_TILER_PRESENT); ptdev->gpu_info.l2_present =3D gpu_read64(ptdev, GPU_L2_PRESENT); + + /* Introduced in arch 11.x */ + ptdev->gpu_info.gpu_features =3D gpu_read64(ptdev, GPU_FEATURES); } =20 static void panthor_hw_info_init(struct panthor_device *ptdev) diff --git a/drivers/gpu/drm/panthor/panthor_regs.h b/drivers/gpu/drm/panth= or/panthor_regs.h index 48bbfd40138c..8bee76d01bf8 100644 --- a/drivers/gpu/drm/panthor/panthor_regs.h +++ b/drivers/gpu/drm/panthor/panthor_regs.h @@ -70,6 +70,9 @@ #define GPU_PWR_OVERRIDE0 0x54 #define GPU_PWR_OVERRIDE1 0x58 =20 +#define GPU_FEATURES 0x60 +#define GPU_FEATURES_RAY_INTERSECTION BIT(2) + #define GPU_TIMESTAMP_OFFSET 0x88 #define GPU_CYCLE_COUNT 0x90 #define GPU_TIMESTAMP 0x98 diff --git a/include/uapi/drm/panthor_drm.h b/include/uapi/drm/panthor_drm.h index e1f43deb7eca..467d365ed7ba 100644 --- a/include/uapi/drm/panthor_drm.h +++ b/include/uapi/drm/panthor_drm.h @@ -327,6 +327,9 @@ struct drm_panthor_gpu_info { =20 /** @pad: MBZ. */ __u32 pad; + + /** @gpu_features: Bitmask describing supported GPU-wide features */ + __u64 gpu_features; }; =20 /** --=20 2.49.0 From nobody Sun Oct 5 05:29:01 2025 Received: from OSPPR02CU001.outbound.protection.outlook.com (mail-norwayeastazon11013061.outbound.protection.outlook.com [40.107.159.61]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id 4257726FA6A for ; Thu, 7 Aug 2025 16:27:52 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=fail smtp.client-ip=40.107.159.61 ARC-Seal: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584076; cv=fail; b=FVkZVvSMoFrkUMVlbYdANHAdIoC1uLGfHgFvRq6jN1rQT2VVCPXprCJrs++i75udk2awA6L7QA0Pvo8lf6XY+x7pUC+XFSqmNqoS/WP1HJPKPiNKqN3GIS4OfNp7XI0crKvVXzqAVeOwTiNjzcKcQ0PGN/XuVVwRw4m783WFYtE= ARC-Message-Signature: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584076; c=relaxed/simple; bh=Cgm5RAxrot86ODE/Fu/+JveWB2FCo/AmetV1ToLQ33k=; h=From:To:Cc:Subject:Date:Message-ID:In-Reply-To:References: Content-Type:MIME-Version; b=eREizuG2+81Dms/ADe1UEocIRAYYjFYAJe79zmiUz6qiY6C1BXJ2MfsAcG1WvmQXygPZF1xNAL2miBlG4h+KV65/Bb1xYPOm3l/MZHHAavhZVIinkkabVPr6xKxx8Xhn7UYqeHN9TH0LpxE+rptZwVf+SYq4If2QIHUseo+cpsY= ARC-Authentication-Results: i=3; smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com; spf=pass smtp.mailfrom=arm.com; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=RWrX8PFc; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=RWrX8PFc; arc=fail smtp.client-ip=40.107.159.61 Authentication-Results: smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com Authentication-Results: smtp.subspace.kernel.org; spf=pass smtp.mailfrom=arm.com Authentication-Results: smtp.subspace.kernel.org; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="RWrX8PFc"; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="RWrX8PFc" ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=gKXdmhMqU8VM6EDAPBTA7BChMNMgbmgYDrV62J9uA45Kwxx033QttKeYEkhlizm/y2p2CNLcoSDknrDuwZAr2SaK+FfwMj6b/LhfvirIUL0U6sXS+1vfdX9XR/nub7p5Ib7yIHVqFFXld/zd3PA8zl/vFcteHlGsD2vv4ZhiU+AbK0/7UeqegO9pCt6TwzYNdranzoa2v2B5X5ayfXGa0MIIL9QoHzgOFYSoyQ8HBkyVUyd6HLgvu7o6OHCCEXJMHGeKWNPUjdgIYIBlHDMvnprMoxLiPCvWy2Bqme1Z0XqNkA1HGbdij5sutXjTvLX9rkGIXe2hElDdkX4tR4uPlQ== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=3cX0lVxuc3vcustMH6MsbS4CtipjD5IDpDsg7l0aUso=; b=K9U8kdOocuhmgqNeHxYurUK8XPFu6HNgJbPlg9h/uW3E28CAahbFnvLAQEapd+xj3pVN9VzaZ2KdPrxziVTtueqVmkmtiJxBNi4aCNgtrErRuOGkJdY1IdW1LL4KZwJsoNJ+qgx153jxJ7gSruOpSR4zhrP3f8KLPILfyNSo15Yt672z1MXHiOkor2kd3rQk7U4fcm/AXx776Bev2hmlMvIitDuL57kGTruiZxFFH3tUypA16Y2z2iZxOpyGmJg7C6GPleK6cwc9Ov4iEYSQSlRQ5HpXRnJvAKWBgYOj/Y6A1ceu85Fd4MGngQjOFGQzyMX2NfyHVtaKbfCdjCdOzQ== ARC-Authentication-Results: i=2; mx.microsoft.com 1; spf=pass (sender ip is 4.158.2.129) smtp.rcpttodomain=lists.freedesktop.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=pass (signature was verified) header.d=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=3cX0lVxuc3vcustMH6MsbS4CtipjD5IDpDsg7l0aUso=; b=RWrX8PFci0kI3Q/H+JHCDSoZn5AxontxyGjTrT16zIHhn+8o1lDVsCkY6EYD6v2i7rTT3aeS0ZSAyg6CVyXpDU2STJyAggRMAzK02NY5VHgyiOxERE6VDUZaHQrdL9NiE91gfosrT0xI3XIorYmQtIKFwJ5sI2uv37/B6dp2C0Q= Received: from AM6PR05CA0004.eurprd05.prod.outlook.com (2603:10a6:20b:2e::17) by AS8PR08MB5943.eurprd08.prod.outlook.com (2603:10a6:20b:23e::10) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.14; Thu, 7 Aug 2025 16:27:49 +0000 Received: from AM4PEPF00027A67.eurprd04.prod.outlook.com (2603:10a6:20b:2e:cafe::57) by AM6PR05CA0004.outlook.office365.com (2603:10a6:20b:2e::17) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.14 via Frontend Transport; Thu, 7 Aug 2025 16:27:49 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 4.158.2.129) smtp.mailfrom=arm.com; dkim=pass (signature was verified) header.d=arm.com;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 4.158.2.129 as permitted sender) receiver=protection.outlook.com; client-ip=4.158.2.129; helo=outbound-uk1.az.dlp.m.darktrace.com; pr=C Received: from outbound-uk1.az.dlp.m.darktrace.com (4.158.2.129) by AM4PEPF00027A67.mail.protection.outlook.com (10.167.16.84) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.8 via Frontend Transport; Thu, 7 Aug 2025 16:27:47 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=RXzkjCqtNOKu7XWfc1at6O42pDCt/4mNAs1HQ21LljDHCChnVSpNRNPMpc27UiNHnyYzde3JpVzFv7XOomABWr73KtwQZEVLpsGH+tME0MHgxtMLcz21iD8Ex26zdjcGztQL5h2vY4/kIyj3hj8qmsDgb/8ro2KTL7muY08+EO8oiszd391b9o+kVDOsj6wbCDE/zhFsR7qiyqopYUMlPkOI3RveANxIG+vWDf84QBqWtHPH9Vpof4KBKyqTqHXeY4Z9tsjppNA93QlHailghBgmtbtXVAEfQFBYnXZH7WXBwt/BWKV6Xf8Xa9PIcScPF0frhez6tfQ9qKfm069tgg== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=3cX0lVxuc3vcustMH6MsbS4CtipjD5IDpDsg7l0aUso=; b=SQ2VfQyf/eLuNTtGWrpE7MtAm5FhWrtR3wjCXXYWAy4MSwrNtE6oVKqJnTE9LYCzXWZyGfek7XoCJAHJ8/yiSvhueJE6mG5lie4W8oH3pvxRKk80GDXmb1eHp6AnOXuHpCeEiGqZtdli6sG0XRSDnk69XLeIbOFcgW2YZCA8Wf4T/efbHC+pQaWmUWK9wdzdN1IUf2cOnea+qsVXL4EgFvuh+nHBbKsbHE5cVRegh3hkvmzrj5MZjc5PLCjZstLPiCRWu3qaRNxoPUM3bWwTk+6+Ct89OnLS9ZaEwJeyslX4QArgNVlScW6bSWcLKsjBisR/urGxslRYt4yfbgLevQ== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=3cX0lVxuc3vcustMH6MsbS4CtipjD5IDpDsg7l0aUso=; b=RWrX8PFci0kI3Q/H+JHCDSoZn5AxontxyGjTrT16zIHhn+8o1lDVsCkY6EYD6v2i7rTT3aeS0ZSAyg6CVyXpDU2STJyAggRMAzK02NY5VHgyiOxERE6VDUZaHQrdL9NiE91gfosrT0xI3XIorYmQtIKFwJ5sI2uv37/B6dp2C0Q= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) by DB9PR08MB9443.eurprd08.prod.outlook.com (2603:10a6:10:45b::19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.13; Thu, 7 Aug 2025 16:27:15 +0000 Received: from VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74]) by VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74%5]) with mapi id 15.20.9009.016; Thu, 7 Aug 2025 16:27:15 +0000 From: Karunika Choo To: dri-devel@lists.freedesktop.org Cc: nd@arm.com, Boris Brezillon , Steven Price , Liviu Dudau , Maarten Lankhorst , Maxime Ripard , Thomas Zimmermann , David Airlie , Simona Vetter , linux-kernel@vger.kernel.org, Dennis Tsiang Subject: [PATCH v9 5/7] drm/panthor: Serialize GPU cache flush operations Date: Thu, 7 Aug 2025 17:26:31 +0100 Message-ID: <20250807162633.3666310-6-karunika.choo@arm.com> X-Mailer: git-send-email 2.49.0 In-Reply-To: <20250807162633.3666310-1-karunika.choo@arm.com> References: <20250807162633.3666310-1-karunika.choo@arm.com> Content-Transfer-Encoding: quoted-printable X-ClientProxiedBy: LO2P265CA0285.GBRP265.PROD.OUTLOOK.COM (2603:10a6:600:a1::33) To VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) Precedence: bulk X-Mailing-List: linux-kernel@vger.kernel.org List-Id: List-Subscribe: List-Unsubscribe: MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: VI0PR08MB11200:EE_|DB9PR08MB9443:EE_|AM4PEPF00027A67:EE_|AS8PR08MB5943:EE_ X-MS-Office365-Filtering-Correlation-Id: f1e42d3c-7ef2-4dca-d216-08ddd5cf58bf X-LD-Processed: f34e5979-57d9-4aaa-ad4d-b122a662184d,ExtAddr,ExtAddr x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|376014|366016|1800799024; X-Microsoft-Antispam-Message-Info-Original: =?us-ascii?Q?1viBti3kIBmQxYe8XABluHeuWApEjjNdpgZWg1YIlouTiBEbiO+s2CYmYbgY?= =?us-ascii?Q?twoCL51hECaYvypZql9PFPwid022oLgsGJllLiLf0ii78BHlLqxEy6iHXHU5?= =?us-ascii?Q?7Ac52JbU7iw6+Ebjq/rdGJiWCHmHZZ0GRRtpd8Lva9rOCLQbybDtARrhygzL?= =?us-ascii?Q?YGU6KSEfnp1Z41HLwoI4qg+VXoymUWuARympzF7ckP2BhqrTh3oXzdSmimt0?= =?us-ascii?Q?YASgSbV44FyNRwOovbKtJsQV5b/f8kyDq2cdjPGcLvWUeqSrghF4J/7XrGPG?= =?us-ascii?Q?DCNuSF2a5fGTcgQMuaxbefJMSEuN2a/0InIzi6Efw476W7Bs/ELJh73K9WRp?= =?us-ascii?Q?Hx7AOE4pn4mAk8e3jmvTnD5e9ZpkC/oYfWlrHOYiH4+om4lL5WT6XPrnpO2f?= =?us-ascii?Q?R1aUOW3M8LJrqNlzw56YioM9ajLNxruRMVfHhAleIWEWtDdDOCdD81HLnXix?= =?us-ascii?Q?C/l1h5LgJ1d9PRlRo1zFjOw9NREr2qXvV5f6BM9wMZC9a5lQ0MKDlrZVAop8?= =?us-ascii?Q?CiYvJH8uwmRNe1NHq5pyLxJKmAuIuW/0JlGSqgmFvDxjtDF8CzdQODcrF4Ay?= =?us-ascii?Q?818koypH9nnQxpiNkZD7F5dSQ5NVtorOxrGsuZgzWmJlJJnFwmAMkj/87X+I?= =?us-ascii?Q?Gl/ClvniVlma8CuNjVhD6KIIw2vYo7ZEabd3hHdPM86qtANTQFUe68NvUOPl?= =?us-ascii?Q?OcmRAiGvsoHeAbpt5XogpRogPP8esYYDrHdWhWJRFc+x0ivQadiz3IrozKRc?= =?us-ascii?Q?1hmsvacbjE/t25cMsGTM3yXA4UhmIWf04+1uZI5nedudqcFJyZdAcpFB8OYA?= =?us-ascii?Q?CpLp+ZFsZw8UQdZoGyiBGUk7O58x1pUSbKILzcQpuorBue1reeY7OQd12XHJ?= =?us-ascii?Q?bK8JD9TIo/StXWcSqTPg27K2Zh6UWXXL3IH52CrDncxDTrAV+o3d1ZtlSUs6?= =?us-ascii?Q?aala13XQ7gmP0qZH3bDRMcxxRkPefFnzEno8QpbE+TrOAI9Yth6VypKNXoId?= =?us-ascii?Q?7/jZK1idU3a0UTh1nY6WwSgDUQnNm2a7MWatS8w9kWUJHKbL9hdR+aGLry/8?= =?us-ascii?Q?O3ba8c17LAyP1GFQ7ZZ0yZbbKdc61R7/EIqQfJ907p2YtNfT+6cP0qI6Ehvw?= =?us-ascii?Q?IQuPOLXPFHlkL1vJQ0HmBHcIULm9VI4Kzz9bKXxj8KmktG/iqK8ORgtqnzzH?= =?us-ascii?Q?6wfjHy9c8SCwNlk5nMNkCuienVzG+5QBiii1rrwsorSQmgybmlUimJVImHfh?= =?us-ascii?Q?07wZKYgJihMMci8mSeCkF8J23Lssj9GbWuGOAoj3+sxitbo27HiZmqGB+qa5?= =?us-ascii?Q?PY66jLaTZirIhbN7Ad6ETJ01nxdjlpRuofHijV4g2GUfDEtC7nn2DUeCkBac?= =?us-ascii?Q?isRLV4n2ezgzosnnsayfEkfPJIf8nJcO6ntJnRUpm3jxI4Io42MZXk7H1cHV?= =?us-ascii?Q?KEGmdNZ4eEk=3D?= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255;CTRY:;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:VI0PR08MB11200.eurprd08.prod.outlook.com;PTR:;CAT:NONE;SFS:(13230040)(376014)(366016)(1800799024);DIR:OUT;SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB9PR08MB9443 X-EOPAttributedMessage: 0 X-MS-Exchange-Transport-CrossTenantHeadersStripped: AM4PEPF00027A67.eurprd04.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 4a51f9a7-d502-4f12-fdec-08ddd5cf4569 X-Microsoft-Antispam: BCL:0;ARA:13230040|1800799024|35042699022|36860700013|376014|82310400026|14060799003; X-Microsoft-Antispam-Message-Info: =?us-ascii?Q?wnP/tgdWofVWOH7i/rdDei/wxxGXUacw2jThOOM5giVSl1rhCcwW7+jTTOTE?= =?us-ascii?Q?Le1cqTpu94dZsoY5oLS5xiAv721gcKuV35/niVJcdheBxkHBf1h5jDROUgsX?= =?us-ascii?Q?30o/ByfzVlMB0aeWidEfaSuCtxlsEzgPC1ke0NH/tFfI4++6pn6YcVzS2m8y?= =?us-ascii?Q?/yibCefVOt7F0xYM3P/0MnmaqBV1s6LecP2nMKGQVqHBJmKEQUnIKvXnZDbE?= =?us-ascii?Q?95PC+yOxgN59fix1MPmiljp3wdOeyPENCldeB7V4dk7GWzfbW3z0lpWmVtMU?= =?us-ascii?Q?5bKR2khe2lGDQPN6Zrwc98r1eUP8W1JAkH+xdSdyweWETCGLjyMoZkJ+uw7A?= =?us-ascii?Q?1bz6gtXdZFOXAJ2Lo+Qrc4jwWS77Tg5NKez8csWYxOeI1UIbmsYtyfwCaqh+?= =?us-ascii?Q?QDGb/y23Gx4rEpULl8TM2mrfApqv7foa3tShsjgqGVocmxSfQibAGhYw9QxD?= =?us-ascii?Q?aQbRw9DXGhqsPT3GGseYYqTqtNE+OVTKbWU+Lc/0a9Et2ooKPKmHDTaxWBwV?= =?us-ascii?Q?gztdRUHhPuxdLcZRqXQMyJ2WKVcq6oLOh+/LTyWa9nYxI5fXbJAzMUyNSGpg?= =?us-ascii?Q?3yrpGgmHNdxp/ehgPwOEJnRcSzZ0KO7r+oNG+TXL86vorPa3tHp/Jt9OtztO?= =?us-ascii?Q?CbxK/iQf3LmU21ZeXPHIewnXVnksFy1+2Gd3dbiT+hV7yIED5zO4hWrnkQP/?= =?us-ascii?Q?SKyM0u3k1eSV7YJlD0QklVYORjCQ1YGYCKqhOzAMRGG4CxwDPwz51z9HXD47?= =?us-ascii?Q?fRDE5zTBHoJtNUaG0vCjkhHkU1NPsj/TpVbasZah9TKhmDRLHwy/sIkhbx6Y?= =?us-ascii?Q?oFRLNK8ttaYds1I4X1OBJ+LQpxtTcgsKttbwUJGXioFeKGg3XzRFZvhRjcBG?= =?us-ascii?Q?DcekcRUxyWZYjp+j8VzTL7ampFZaNwjaAN9ef6CuNKKtVdLo8QnshZ875pV5?= =?us-ascii?Q?FpuMEyhAhd5wz6bzba1kv1vLFttSmWwgL6jf+EDtLEsONRRtVFwAe5HWoDC2?= =?us-ascii?Q?PAYXoZpuNOwJKq+hUJ8mEomokMTfvTb73pk83BFssixmNSZH0ky8tgkker3T?= =?us-ascii?Q?qGJUXFR0FaZlAq0OVcueQB9JqEHGuxP/5dhyWsa/Vhv33zWrnB42IYYqBY4z?= =?us-ascii?Q?QAr4IxJ/nXZrlQJWU3vJIEnMtRQklIAYbK8gJxSmtztIgzV1C3uyRksFJUcv?= =?us-ascii?Q?USqqsFrqC0cE5OgfcP729o8Dy21JJXI1s4TNjlp/EdCdqkFX1ZJZEXKov/CX?= =?us-ascii?Q?DAwppnKxTz0j6GC7iQ831UfVj2TaRcRqmFQPDL17l9TR/VtWhITHpjfnL6ut?= =?us-ascii?Q?06F9gPzoUkOEgr8HglmHS5vdEoXHI2ZOKL3jI7f5r7IhaHTRCyVcPaHBPM32?= =?us-ascii?Q?vbR6Wjo92UHLdZfGUhW/9sdMRWHd7wvyaVlNLZ5NSon2ZwuMWkXVpoZ+Gb28?= =?us-ascii?Q?eThvqUU1hhfWF3Oqw7lFAF0fkG3b3sfwaCrLYAcpxm7KFbKl05kEtWznhn4x?= =?us-ascii?Q?MF3gKjyx1AGeLvzHeHsti7jF+gskudRymEwq?= X-Forefront-Antispam-Report: CIP:4.158.2.129;CTRY:GB;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:outbound-uk1.az.dlp.m.darktrace.com;PTR:InfoDomainNonexistent;CAT:NONE;SFS:(13230040)(1800799024)(35042699022)(36860700013)(376014)(82310400026)(14060799003);DIR:OUT;SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 07 Aug 2025 16:27:47.9537 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: f1e42d3c-7ef2-4dca-d216-08ddd5cf58bf X-MS-Exchange-CrossTenant-Id: f34e5979-57d9-4aaa-ad4d-b122a662184d X-MS-Exchange-CrossTenant-OriginalAttributedTenantConnectingIp: TenantId=f34e5979-57d9-4aaa-ad4d-b122a662184d;Ip=[4.158.2.129];Helo=[outbound-uk1.az.dlp.m.darktrace.com] X-MS-Exchange-CrossTenant-AuthSource: AM4PEPF00027A67.eurprd04.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS8PR08MB5943 Content-Type: text/plain; charset="utf-8" In certain scenarios, it is possible for multiple cache flushes to be requested before the previous one completes. This patch introduces the cache_flush_lock mutex to serialize these operations and ensure that any requested cache flushes are completed instead of dropped. Reviewed-by: Liviu Dudau Co-developed-by: Dennis Tsiang Signed-off-by: Dennis Tsiang Signed-off-by: Karunika Choo Reviewed-by: Steven Price --- drivers/gpu/drm/panthor/panthor_gpu.c | 7 +++++++ 1 file changed, 7 insertions(+) diff --git a/drivers/gpu/drm/panthor/panthor_gpu.c b/drivers/gpu/drm/pantho= r/panthor_gpu.c index 5e2c3173ae27..db69449a5be0 100644 --- a/drivers/gpu/drm/panthor/panthor_gpu.c +++ b/drivers/gpu/drm/panthor/panthor_gpu.c @@ -35,6 +35,9 @@ struct panthor_gpu { =20 /** @reqs_acked: GPU request wait queue. */ wait_queue_head_t reqs_acked; + + /** @cache_flush_lock: Lock to serialize cache flushes */ + struct mutex cache_flush_lock; }; =20 #define GPU_INTERRUPTS_MASK \ @@ -110,6 +113,7 @@ int panthor_gpu_init(struct panthor_device *ptdev) =20 spin_lock_init(&gpu->reqs_lock); init_waitqueue_head(&gpu->reqs_acked); + mutex_init(&gpu->cache_flush_lock); ptdev->gpu =3D gpu; =20 dma_set_max_seg_size(ptdev->base.dev, UINT_MAX); @@ -258,6 +262,9 @@ int panthor_gpu_flush_caches(struct panthor_device *ptd= ev, bool timedout =3D false; unsigned long flags; =20 + /* Serialize cache flush operations. */ + guard(mutex)(&ptdev->gpu->cache_flush_lock); + spin_lock_irqsave(&ptdev->gpu->reqs_lock, flags); if (!drm_WARN_ON(&ptdev->base, ptdev->gpu->pending_reqs & GPU_IRQ_CLEAN_CACHES_COMPLETED)) { --=20 2.49.0 From nobody Sun Oct 5 05:29:01 2025 Received: from DUZPR83CU001.outbound.protection.outlook.com (mail-northeuropeazon11012055.outbound.protection.outlook.com [52.101.66.55]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id 7B9E42701D2 for ; Thu, 7 Aug 2025 16:27:57 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=fail smtp.client-ip=52.101.66.55 ARC-Seal: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584080; cv=fail; b=th8GtpW8clsqyv0uR/3W4dPXa80CiEqg7YqdVTuzX+FQCkxzg8Y6ipC8ah3e97uDTpiBifPKdOVIqR0WqK9GyeLd7ze2LcvH1Y2BPx+iHMZlJc6pAbwulS5OI8LRJMejIQguvv8x/dVtZHbdgTckXHPSHCd5vw+IJS4q5bvalHY= ARC-Message-Signature: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584080; c=relaxed/simple; bh=TkKn7i/UppWvonDkWpHVvsY8aThMWRkOCVkH06rJhfo=; h=From:To:Cc:Subject:Date:Message-ID:In-Reply-To:References: Content-Type:MIME-Version; b=R/Usb1N1Zlbp1OvFF7eqZm6lJST2hSx+18sU4Or6Zq7tzEebMiLtQwFl5rBW1M++GaPSuA87Qu/GikB+AdTP/+A7490YQoYHkLLJ6/w4Blv2MG/hqx48LMWtGu2pzCuzq9b4UdBTqOgsgYZfBZdcpcRuS26SZwdNVqJIOpzuKMs= ARC-Authentication-Results: i=3; smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com; spf=pass smtp.mailfrom=arm.com; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=a6dL9YJS; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=a6dL9YJS; arc=fail smtp.client-ip=52.101.66.55 Authentication-Results: smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com Authentication-Results: smtp.subspace.kernel.org; spf=pass smtp.mailfrom=arm.com Authentication-Results: smtp.subspace.kernel.org; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="a6dL9YJS"; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="a6dL9YJS" ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=xSxfEf24JeCQgEQYalI1gVKuY6VBSi9rZyQU2Z5+m6Te5riCVHu6Nsw2APwYbxdvTAx69gjolLt8lg7W2DUrCzeHUDYq9jfjyl+SfugpPyL3DLmUAExPsMa4h2h20vGbOr45G4YnL9L+6UurooElArKoUU8bSqZW7YNPbSdyB7OiuE3TvA12ETbPqefMAbuBhvA25xLs+mmBxo7svn5Sgr/3S9+3WN2+jfW29WngjeGscq2qLL9EvR7dwQjdC3YXTGIrx0xWlcqWTo8z62msY9iLvLCijxBuey4VgAYJRL2N+mKBQM5HdLOIhmTmUZlQOoa1lwBTtG1inTGDyOcgGw== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=hiYRKa+MyPgW8ej7ffMLZsqHEvtEjQVumfPDwjCyGK8=; b=YgRJC9HXyRyLyolmh710Wer/C0nr5P9qSjbD7JD+calUjIemCPWdC5uKTub+jPMAisyt+oklkCss+K/U5sZyLIa7BjBnsPxZshj7LAg1GbCods1sYncMunTSR1kDfQkmavdbCtk6RNN7N2hnmC4WfZtDGjCgTaus1sz2I+ghJzWPI3ZaxHztm+hS6FvbRXgvXz2eQ+6ODriCDI9MNaNWsWcmq5d9xa5ExofwKc49LD9bSeLpfilv2RYgpNoi9BnjGpZU3ufNyXNh3F12tWSlFFjusCAN8h4lH5kmPx6z2P4Wnz8Afk5LfvQtHhmZo6oJB1PWxU+++O1eA3yTvXjX0A== ARC-Authentication-Results: i=2; mx.microsoft.com 1; spf=pass (sender ip is 4.158.2.129) smtp.rcpttodomain=lists.freedesktop.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=pass (signature was verified) header.d=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=hiYRKa+MyPgW8ej7ffMLZsqHEvtEjQVumfPDwjCyGK8=; b=a6dL9YJS9LDGHZEpXFQK1n8y9f5MnXWgVya8U5XVTs2B2tCqqg2rj94LdIVz4k5NNYu6CELabjyd6sX8XEdofO+KOexFpirGSNfZkyYv37D4CoCHb7cs4lYbCCgkXYTYhPHpj98+/4OsAMWOVdQw0sMMuV7tmaiaZ0de5lmF+vY= Received: from DUZPR01CA0007.eurprd01.prod.exchangelabs.com (2603:10a6:10:3c3::11) by AS2PR08MB9103.eurprd08.prod.outlook.com (2603:10a6:20b:5ff::16) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.16; Thu, 7 Aug 2025 16:27:53 +0000 Received: from DU2PEPF0001E9C1.eurprd03.prod.outlook.com (2603:10a6:10:3c3:cafe::8d) by DUZPR01CA0007.outlook.office365.com (2603:10a6:10:3c3::11) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.15 via Frontend Transport; Thu, 7 Aug 2025 16:27:52 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 4.158.2.129) smtp.mailfrom=arm.com; dkim=pass (signature was verified) header.d=arm.com;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 4.158.2.129 as permitted sender) receiver=protection.outlook.com; client-ip=4.158.2.129; helo=outbound-uk1.az.dlp.m.darktrace.com; pr=C Received: from outbound-uk1.az.dlp.m.darktrace.com (4.158.2.129) by DU2PEPF0001E9C1.mail.protection.outlook.com (10.167.8.70) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.8 via Frontend Transport; Thu, 7 Aug 2025 16:27:52 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=qUSA+/90bIEhQ0a7VMRU8SuFF1pX1yNmQnH9WU1iud7X/saT0Zacdv4gQn3zfkkIy+xhNMh1j671ohSQFQ5za70o3ffaW+kjACDz95W+KMoxXDbK1pXKJN9JojlfKJ22QOSPODAyTBpGrELdlknXpqAxfm5cwZa25Xv8S1+YSbONqDOi9tlQ5e5qIESpXtjYhEJR03R+wxjCLym8SQp/jq5hpVxwALG0GzakOIJDvSq7dHeSV+lgcWdnM/ugHSTXvHJA73jnKlhMqmRPdV76hM9JxcWxAEFHlWNvQzxv7k2TlZU1fVbuWmRR7uDDg0zZeXkOHIh6g7YDr7s3QRKqdw== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=hiYRKa+MyPgW8ej7ffMLZsqHEvtEjQVumfPDwjCyGK8=; b=EeOtLhvavhyrjm9TDis7pNBE0rIcWWOHeKndsntUJHiN5jFfmJzG1/hn7eoj1U5VIyqRtGO9It4E6T2+0T5aGlK1YxTw/3U9d2aCDgLioVi3+oVBgkg0pRa5PQdzK7Gnz6tRi1M+3VD6/YmxyljSYBJPiAtPJQAmdavkFy1Uo5vah5wNhbfsc+2fL3pDcg53YmngUmvHtZUd3ToPXaWvhDKNscbzpvgcCG4XqmgQ0cG2uYkhsB/9erWMawbkBbdGKkMXJRVjvWxr8dbbMLXnEIakBKQWrsPwji3tixmh8dfNuqvcJEICwDH5UWqGZjvzLa/1tvjp870l0OEEq8S5/A== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=hiYRKa+MyPgW8ej7ffMLZsqHEvtEjQVumfPDwjCyGK8=; b=a6dL9YJS9LDGHZEpXFQK1n8y9f5MnXWgVya8U5XVTs2B2tCqqg2rj94LdIVz4k5NNYu6CELabjyd6sX8XEdofO+KOexFpirGSNfZkyYv37D4CoCHb7cs4lYbCCgkXYTYhPHpj98+/4OsAMWOVdQw0sMMuV7tmaiaZ0de5lmF+vY= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) by DB9PR08MB9443.eurprd08.prod.outlook.com (2603:10a6:10:45b::19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.13; Thu, 7 Aug 2025 16:27:20 +0000 Received: from VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74]) by VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74%5]) with mapi id 15.20.9009.016; Thu, 7 Aug 2025 16:27:20 +0000 From: Karunika Choo To: dri-devel@lists.freedesktop.org Cc: nd@arm.com, Boris Brezillon , Steven Price , Liviu Dudau , Maarten Lankhorst , Maxime Ripard , Thomas Zimmermann , David Airlie , Simona Vetter , linux-kernel@vger.kernel.org, Chia-I Wu Subject: [PATCH v9 6/7] drm/panthor: Make MMU cache maintenance use FLUSH_CACHES command Date: Thu, 7 Aug 2025 17:26:32 +0100 Message-ID: <20250807162633.3666310-7-karunika.choo@arm.com> X-Mailer: git-send-email 2.49.0 In-Reply-To: <20250807162633.3666310-1-karunika.choo@arm.com> References: <20250807162633.3666310-1-karunika.choo@arm.com> Content-Transfer-Encoding: quoted-printable X-ClientProxiedBy: LO4P123CA0137.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:193::16) To VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) Precedence: bulk X-Mailing-List: linux-kernel@vger.kernel.org List-Id: List-Subscribe: List-Unsubscribe: MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: VI0PR08MB11200:EE_|DB9PR08MB9443:EE_|DU2PEPF0001E9C1:EE_|AS2PR08MB9103:EE_ X-MS-Office365-Filtering-Correlation-Id: cfb2e50a-64e9-4f5e-7b85-08ddd5cf5b4a X-LD-Processed: f34e5979-57d9-4aaa-ad4d-b122a662184d,ExtAddr,ExtAddr x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|376014|366016|1800799024; X-Microsoft-Antispam-Message-Info-Original: =?us-ascii?Q?JXUVmYoYE6ec35ZFEc9WPPvjGeukLZ7jeXi4RFPFg6IQbpf4qrVjtJ3EWWHG?= =?us-ascii?Q?VdhZhueBDKa4hrJyV0Wjd/xG9DbCxjzHGMKGXxub8+7ucSxzZLfscg2ROSJK?= =?us-ascii?Q?9hclPpJYHaLErjF+pWGKIvbnmSJbDRyPOIxpybkJffMv/OGpLYG1GJQjPiVC?= =?us-ascii?Q?ru/BaqU4YGRkmjxJYtT1/Ae8nvMdDWDGcC48EfJsTZ34oRzgFcWnnrmYyNwR?= =?us-ascii?Q?IsqT412HJO/1WbqBMg7zg84RGmTGINnZsed+tplWvWj49ubv+LCY19pp0yZ3?= =?us-ascii?Q?2LF8XuVdjinIHCkcln9eBMRIBPqRrWpCnIe4x0TJ9ypMVcVHBhjZd+7V60/v?= =?us-ascii?Q?hCUdiTFYZ8dOXZfq7jBgST9FcDHP6kjPccOHjcw0qZ1bXK4GlMPsdzxQAGjw?= =?us-ascii?Q?aCn47xoAbTPZJmB27fu/2N8p7szm8hv3YreJDhj2MMq2uOB8KGvUTeTwV/Dy?= =?us-ascii?Q?GEoXno7bnqb/llBvzNppb+dD1vlCVnNyxLpVC969AuWWWErWGW5LJDknCdr/?= =?us-ascii?Q?QdQA/Urf2A9yz4unWumTdWp8I7l7acyPYiclJHtg+gHJtCV4ga8xdYt5ITp3?= =?us-ascii?Q?pYLvNHgMNVPPyHbyLqPHP3TzFtvVu0XCbbbKHdDlEuYnjpWRfyEJpFfydPQe?= =?us-ascii?Q?417e7NEDCZ1BDCd7VaIOAaieMB07MSkDJAuQi3eNZUk1EzR0/BjB7+SjyC4/?= =?us-ascii?Q?X2JJ8j0kAj0u+qNHOTnm9wfpkpT42CXyAxQxmswYu6JdiWWQPwrfI4o8vUDz?= =?us-ascii?Q?e6fqA8HfSXLVO1OF8msvARhZISo3xuXhAJ/nHwSPrzWSDSjnerp5zDBjEgnH?= =?us-ascii?Q?4MAZxhPrGZ0kSqhbEQ1jNA0NvIJ8T1tpE7d18zSSU1cZxOsNQzYoDnX7o04x?= =?us-ascii?Q?TWMlcYDrtlIuYUHYxldarK73tXUQrYYQS7eUD9cIdJKhY7lLRJ7rHje0DEjr?= =?us-ascii?Q?83V3NP5MUE+G1OvL/V3zjmrfG/t9XBixl8RagGxj6ziAcYhiIqelRO5TdmFA?= =?us-ascii?Q?0AYZkm5Igs4bxbeWqFdUC3xcBSjZIuJhFUicJ2rsy48pILld1KSqFeUXMOqA?= =?us-ascii?Q?fC+Y1V9QLAXxiEu3N3sxiELVH2LWDLplDPGymXd+pu3l5dGjlyh2juYUCpKt?= =?us-ascii?Q?+7S/MA00bCLDAHurw4jSPa6goZsLvk9513l3z9mF3Bpd602yvCZinuK0Ziw8?= =?us-ascii?Q?QLJxCEhFNbmOKMjONt//jmnHZLYlMRQtiDPCf2zazhYko72MDKPPhqMgMDrz?= =?us-ascii?Q?mQfgocW3Hv0HnLGLNnb/7ybjUml7AOB3ZLBK5wPjAnR3GJx8OAdI4x5NBKn5?= =?us-ascii?Q?1CVVUvsZ8OOGzaS8QRdUHoybAXabzB98ZsseN/0xw2bhAi+bz0cWBq+0U5r3?= =?us-ascii?Q?TuQUQ03G+OtxeNFTSzuPb0V+MpONZuR1OzGI8ijhX1fBuY/aAw=3D=3D?= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255;CTRY:;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:VI0PR08MB11200.eurprd08.prod.outlook.com;PTR:;CAT:NONE;SFS:(13230040)(376014)(366016)(1800799024);DIR:OUT;SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB9PR08MB9443 X-EOPAttributedMessage: 0 X-MS-Exchange-Transport-CrossTenantHeadersStripped: DU2PEPF0001E9C1.eurprd03.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: 7a5ae2af-4a3f-4c21-f16a-08ddd5cf4815 X-Microsoft-Antispam: BCL:0;ARA:13230040|82310400026|35042699022|14060799003|1800799024|36860700013|376014; X-Microsoft-Antispam-Message-Info: =?us-ascii?Q?ChaC16NJ9hGmPKtmrYp69M/UNvlv1PfcAnS8VCda77Z4O2PVrAOTyYkaF8U9?= =?us-ascii?Q?hfEMaM0v1Vldy2mWYNYvtcBK+ekRhhd8DsuTiCF4twcbwAq7VC6gLvE0SRPL?= =?us-ascii?Q?w+8yIU0SN/jTT1qySa0F79OxsoxUCoxEy6ER5Ul2UoWaAyChzPJea1fmcQw5?= =?us-ascii?Q?UqfFhaAa4Mve69o+lDy45WnlQC8qcN9dlrR2RNAFy84Ywxf6Tl3645ghQPUS?= =?us-ascii?Q?rNcJ5iIrscTAfXluaLMU5MhIfyuNjcWVGvX00An5WWnVsmtJgfzAYOjWmT1a?= =?us-ascii?Q?RyOyGtVgJev0My77isKHTMhFEtGRwIO23mr5/pjA7xx9KI/YNmf+qvyTmo16?= =?us-ascii?Q?AhPJeyZuLKR/qlDJlC3YEC8YVJiah+87N8eKwkPjSmNaxtOBRJfMvgBZJFHU?= =?us-ascii?Q?gJtnVX/iiLQvTbvPz/fj9LGP1DQRdFPtqO7TFgMF260vwNueJHIH6V14IjZC?= =?us-ascii?Q?U9+6gCtnrFsjp7mly7a+hVXf+Q1jagYao2cRBpHofVd+UIfKf+19BjyQRBid?= =?us-ascii?Q?T7nPNFPBr+S/eWU1Cc5fzsZYG3k2+AKshRKyKVRccsxhbAL6pM4oksi+XchA?= =?us-ascii?Q?mheLUjF1oqc0n+IsQwBjsIe4FxoHHdnE7pASZh754dPql34ueql5NbaKnSzo?= =?us-ascii?Q?6jeIKWZSI4LWemHGUyucCrALv43PRpD2y/t/haycTEe3gyGMP0zrRmlewFCV?= =?us-ascii?Q?nIJ9xvDQt49ihgRw3c0ilZC0RHXMp4dWkS/OcEKSwgUIYM5LTbEpc1WsbquB?= =?us-ascii?Q?ePYrI0CZwB5aygX3XLPmp2BiWs0UQgJc/Vgn+fsUUvobZyQzO+o3NqaWcSRG?= =?us-ascii?Q?kdhWvwfmMuN8++2cFqmUGeT+SCbgjO3US6yqwLKd+dJCPOs9ulbjw6CNvy4b?= =?us-ascii?Q?5rWbUbTEKpUIA7/BjwyhJbL1IejZ/f5cBo/dDhLWOf/K6m1uZU6zifT8GDml?= =?us-ascii?Q?1Oze7nC/bfrwpF2K0fBDyD4rr31cCDfDiqjHWHu3O7/BrbSuIiBFvYbvCtXG?= =?us-ascii?Q?vJzpyw+zFNeHxdh4nqSjjNHfJ3EUdSf7NZXF/Qr20tCciciyWT8aCeV1UMdM?= =?us-ascii?Q?AXIZmlKCnUQnQu0lgrEdj1d4Xwt9kL086foV0HzdZmbAxsTiZjLCLXL6flJ2?= =?us-ascii?Q?eD6GXiaywsV9lowG8992kpvbzoqx8Kk9vQ3chClNRcwR7fvYWPVUYi454wYU?= =?us-ascii?Q?lBc7yUDIe7u0hO6snZLRlPbvPEyghlrMKu4/53+SdSJgRpX4MjSUxQFqfBj2?= =?us-ascii?Q?yMikYJm+cWwAP26kcOIrslgaqwVmVppO+ky9R1W1A2K9KbgmCRifWisb0VWh?= =?us-ascii?Q?4qiKysA6B+YSkfymgROZGcJygvq9aFV4ASpmC9JtgVuHm5TFNgEr6LRs745P?= =?us-ascii?Q?vLsqCWrvDn57O3U4knLIK2eMUGYetcQLEYen21c/Veg3E0wTd6HsiSaDmDHm?= =?us-ascii?Q?k7ouyCtIzSqtWi0vbOP3KThBWM+z+4gfUqnTRs9uzhxVx38s6MIw5//cy1NA?= =?us-ascii?Q?hjXEaWQywL0X7P0neF5Ldkw+5UfLjm2Si+Ua?= X-Forefront-Antispam-Report: CIP:4.158.2.129;CTRY:GB;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:outbound-uk1.az.dlp.m.darktrace.com;PTR:InfoDomainNonexistent;CAT:NONE;SFS:(13230040)(82310400026)(35042699022)(14060799003)(1800799024)(36860700013)(376014);DIR:OUT;SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 07 Aug 2025 16:27:52.2050 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: cfb2e50a-64e9-4f5e-7b85-08ddd5cf5b4a X-MS-Exchange-CrossTenant-Id: f34e5979-57d9-4aaa-ad4d-b122a662184d X-MS-Exchange-CrossTenant-OriginalAttributedTenantConnectingIp: TenantId=f34e5979-57d9-4aaa-ad4d-b122a662184d;Ip=[4.158.2.129];Helo=[outbound-uk1.az.dlp.m.darktrace.com] X-MS-Exchange-CrossTenant-AuthSource: DU2PEPF0001E9C1.eurprd03.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: AS2PR08MB9103 Content-Type: text/plain; charset="utf-8" As the FLUSH_MEM and FLUSH_PT MMU_AS commands are deprecated in GPUs from Mali-Gx20 onwards, this patch adds support for performing cache maintenance via the FLUSH_CACHES command in GPU_COMMAND in place of FLUSH_MEM and FLUSH_PT commands. Mali-Gx10 and Mali-Gx15 GPUs also has support for the FLUSH_CACHES command and will also use this by default going forward. Reviewed-by: Steven Price Reviewed-by: Chia-I Wu Reviewed-by: Liviu Dudau Signed-off-by: Karunika Choo --- drivers/gpu/drm/panthor/panthor_mmu.c | 33 +++++++++++++++++++++++++++ 1 file changed, 33 insertions(+) diff --git a/drivers/gpu/drm/panthor/panthor_mmu.c b/drivers/gpu/drm/pantho= r/panthor_mmu.c index 4140f697ba5a..367c89aca558 100644 --- a/drivers/gpu/drm/panthor/panthor_mmu.c +++ b/drivers/gpu/drm/panthor/panthor_mmu.c @@ -29,6 +29,7 @@ =20 #include "panthor_device.h" #include "panthor_gem.h" +#include "panthor_gpu.h" #include "panthor_heap.h" #include "panthor_mmu.h" #include "panthor_regs.h" @@ -568,6 +569,35 @@ static void lock_region(struct panthor_device *ptdev, = u32 as_nr, write_cmd(ptdev, as_nr, AS_COMMAND_LOCK); } =20 +static int mmu_hw_do_flush_on_gpu_ctrl(struct panthor_device *ptdev, int a= s_nr, + u32 op) +{ + const u32 l2_flush_op =3D CACHE_CLEAN | CACHE_INV; + u32 lsc_flush_op =3D 0; + int ret; + + if (op =3D=3D AS_COMMAND_FLUSH_MEM) + lsc_flush_op =3D CACHE_CLEAN | CACHE_INV; + + ret =3D wait_ready(ptdev, as_nr); + if (ret) + return ret; + + ret =3D panthor_gpu_flush_caches(ptdev, l2_flush_op, lsc_flush_op, 0); + if (ret) + return ret; + + /* + * Explicitly unlock the region as the AS is not unlocked automatically + * at the end of the GPU_CONTROL cache flush command, unlike + * AS_COMMAND_FLUSH_MEM or AS_COMMAND_FLUSH_PT. + */ + write_cmd(ptdev, as_nr, AS_COMMAND_UNLOCK); + + /* Wait for the unlock command to complete */ + return wait_ready(ptdev, as_nr); +} + static int mmu_hw_do_operation_locked(struct panthor_device *ptdev, int as= _nr, u64 iova, u64 size, u32 op) { @@ -585,6 +615,9 @@ static int mmu_hw_do_operation_locked(struct panthor_de= vice *ptdev, int as_nr, if (op !=3D AS_COMMAND_UNLOCK) lock_region(ptdev, as_nr, iova, size); =20 + if (op =3D=3D AS_COMMAND_FLUSH_MEM || op =3D=3D AS_COMMAND_FLUSH_PT) + return mmu_hw_do_flush_on_gpu_ctrl(ptdev, as_nr, op); + /* Run the MMU operation */ write_cmd(ptdev, as_nr, op); =20 --=20 2.49.0 From nobody Sun Oct 5 05:29:01 2025 Received: from AM0PR02CU008.outbound.protection.outlook.com (mail-westeuropeazon11013071.outbound.protection.outlook.com [52.101.72.71]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id 39CB9272807 for ; Thu, 7 Aug 2025 16:27:59 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=fail smtp.client-ip=52.101.72.71 ARC-Seal: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584082; cv=fail; b=pv5Yg4+0JXZW2BZzTSY2HOCg6xrLLufv1Cv7n77D+HYHfZNA9lTvFd8y+lbWNNwWGUJQA/RM27jvSxOc+Ts88iHb8/phGr2DisfihRWy9wR7UYucpAa7lmYOydbqkPI9QsZAojKOWKgxzlAv0cwteqx37ee1KeCs24qiRPz5/Lo= ARC-Message-Signature: i=3; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1754584082; c=relaxed/simple; bh=ZwZVCfh0wORYMRwn4FZU62xbJ03fgOE/Rd3UY9clDVs=; h=From:To:Cc:Subject:Date:Message-ID:In-Reply-To:References: Content-Type:MIME-Version; b=u3sHO7wpKUWSG0EcIHes69+wJTElOlHcrsQXyiODLOhjPUhP4hEmu9nQToV2XNSpjlHrh/k0tSFYp3fAJUA4cKTrJa0O1g2W+XNfhcCqp0xRlHRi3AnHGOmGi0K177JaOpbhAfbRQpUv1l9haJi1y5J1RsuBDHyRsA9fpQ6OHSE= ARC-Authentication-Results: i=3; smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com; spf=pass smtp.mailfrom=arm.com; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=d6Pc9UnH; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b=d6Pc9UnH; arc=fail smtp.client-ip=52.101.72.71 Authentication-Results: smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=arm.com Authentication-Results: smtp.subspace.kernel.org; spf=pass smtp.mailfrom=arm.com Authentication-Results: smtp.subspace.kernel.org; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="d6Pc9UnH"; dkim=pass (1024-bit key) header.d=arm.com header.i=@arm.com header.b="d6Pc9UnH" ARC-Seal: i=2; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=pass; b=YjiWWAv8mVEuyZua5l0dVK6rGVoZp03HRvJDHOarbAQG2jLEHAN9LEuuoe2VASWgf4n8KVwGopJfV1RHL91iQP3TcPbZP8NVLfgapjkPHOHdmSLnVcx9hf0IvHmCdAc9ddyLjG5plSQkO5LauYxOVWfj+2E48vF42ekXbE66FhYDxm6/FVAhkW8OmfsBDbJVAd1ncY7agNq59y7Sy10M3VAFDylYi1TI6FEtFst2EA6KaIfA5liyOSv/LuaQjrvY7JkZcj81iVIzvJgJUK/dlOr2wyEN2J5OJ1zXfR3o0DKwA2boLE4Z4VGkjKt2acQKErEdqwg6jhaExD3dmmSnPw== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=UUs28UoSJOnec1LakISrYkPOT7k6uFeYEAAL0w78y2U=; b=Ud8M9Pi3LxN4boJdNeUW+/G+VVeopJ+kjujJpQAhH8uoxyX6Nijj11sAyNgzZEx5kPA4YORFbmTAGOuURWKp9zfZYFOqBFzOAqZwCjYZenbCI+NQQpkDAbjfULJeg7BURKrlcy5bkBkrk2/w6VLzWOuHSO1NPnz7F0W4YlqEZPHZMCLer5XocE+fZTiyrs+sYOXLnBt/p88bTqkgu70rUFuWjinE5cjTZboFvKzXPURA/ZOgYpN6gtn68XaH28Ib9hQkUMtheEA2joz/8R1QrRFpqJlGVwuBYwDs2lSjPu7GVnr+GvOWlYhFJ6RerDV9HgUVomUNCFT2n3VsPFFfcg== ARC-Authentication-Results: i=2; mx.microsoft.com 1; spf=pass (sender ip is 4.158.2.129) smtp.rcpttodomain=lists.freedesktop.org smtp.mailfrom=arm.com; dmarc=pass (p=none sp=none pct=100) action=none header.from=arm.com; dkim=pass (signature was verified) header.d=arm.com; arc=pass (0 oda=1 ltdi=1 spf=[1,1,smtp.mailfrom=arm.com] dkim=[1,1,header.d=arm.com] dmarc=[1,1,header.from=arm.com]) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=UUs28UoSJOnec1LakISrYkPOT7k6uFeYEAAL0w78y2U=; b=d6Pc9UnHe32PKe4PV1ealuuOY+MFot5oYfKLpH73Q3L6KbDwigPc2ruzPDSLHQVLplHnA25NHrZ2pHQyRRdVBu0VrY8KXY9zfxGSEQ/O2p3Itrs4pbi9i5HzvWMgjxlvRdaXQh3Zfxu4z3yoegWTA5BMP8fOSRlJEdNQZ/8fD5I= Received: from AM8P251CA0013.EURP251.PROD.OUTLOOK.COM (2603:10a6:20b:21b::18) by DU0PR08MB9201.eurprd08.prod.outlook.com (2603:10a6:10:415::10) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.14; Thu, 7 Aug 2025 16:27:56 +0000 Received: from AM3PEPF0000A78E.eurprd04.prod.outlook.com (2603:10a6:20b:21b:cafe::c8) by AM8P251CA0013.outlook.office365.com (2603:10a6:20b:21b::18) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.16 via Frontend Transport; Thu, 7 Aug 2025 16:27:56 +0000 X-MS-Exchange-Authentication-Results: spf=pass (sender IP is 4.158.2.129) smtp.mailfrom=arm.com; dkim=pass (signature was verified) header.d=arm.com;dmarc=pass action=none header.from=arm.com; Received-SPF: Pass (protection.outlook.com: domain of arm.com designates 4.158.2.129 as permitted sender) receiver=protection.outlook.com; client-ip=4.158.2.129; helo=outbound-uk1.az.dlp.m.darktrace.com; pr=C Received: from outbound-uk1.az.dlp.m.darktrace.com (4.158.2.129) by AM3PEPF0000A78E.mail.protection.outlook.com (10.167.16.117) with Microsoft SMTP Server (version=TLS1_3, cipher=TLS_AES_256_GCM_SHA384) id 15.20.9009.8 via Frontend Transport; Thu, 7 Aug 2025 16:27:55 +0000 ARC-Seal: i=1; a=rsa-sha256; s=arcselector10001; d=microsoft.com; cv=none; b=OZ00DAfa3AHBLgnsZkhdwEJxqaOClTSF1X2x0m/wFyWwccgcKXy1CdqgHi4kj7HMS6GHRynPnCVtgpmwA4ggEiQ/KLAogQmn3S6lzFOVLAWSTLSeHYOC7ZOgKCi+3Si5mHPo1Nd2RbGqqMjBeaWZWsxmVXh/N0o1fpdovkdAkeMCVMbbP52wd2KDIfvFqHIMvboAe4Kc09/tOFyMg3Zxjk1MMtEG6EnD4dKo1qgKl/v0SNgX2jNsU76I2hPO7SOVD4t8oR1hp2Xt0wp7oP7IbykSIrKoSOR7B2M7bg22jAGmYJeH20qz1WN6K8uZw/D/EoobkvfeMI08/miJWLxksg== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=microsoft.com; s=arcselector10001; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-AntiSpam-MessageData-ChunkCount:X-MS-Exchange-AntiSpam-MessageData-0:X-MS-Exchange-AntiSpam-MessageData-1; bh=UUs28UoSJOnec1LakISrYkPOT7k6uFeYEAAL0w78y2U=; b=vqUshTLfjP6k4ExEzVRdxbxpESSAQHSsNG7MLE1ezKVvQ14f6WHGeJoj1Zp0Mo0SvMi9Yc+QTzfTYTKFmQxF+FyWk5n29TNVSQm/tYEJfZqpKTXQSecly1btJ3Yaa+5jba9Pst762Yb1p9K8ov+Fzp+i7B1itPxOZlQfixNcZIXv8ifjY+QUFiTkcsqXvtqhCT1SxISwpvuizY/j9QBqeYh4QrU8LzQNHNuTOz8qFPySH2GVN2AUimpQ6aWlx91J2o/aX4sCrrv52ROdUCVZV2bjxpKF2DMKqcWW0bFlXEtiwWuKnvWWL4gyznakaNu6mkU1/jqTHDbGeNZuecUNHg== ARC-Authentication-Results: i=1; mx.microsoft.com 1; spf=pass smtp.mailfrom=arm.com; dmarc=pass action=none header.from=arm.com; dkim=pass header.d=arm.com; arc=none DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=arm.com; s=selector1; h=From:Date:Subject:Message-ID:Content-Type:MIME-Version:X-MS-Exchange-SenderADCheck; bh=UUs28UoSJOnec1LakISrYkPOT7k6uFeYEAAL0w78y2U=; b=d6Pc9UnHe32PKe4PV1ealuuOY+MFot5oYfKLpH73Q3L6KbDwigPc2ruzPDSLHQVLplHnA25NHrZ2pHQyRRdVBu0VrY8KXY9zfxGSEQ/O2p3Itrs4pbi9i5HzvWMgjxlvRdaXQh3Zfxu4z3yoegWTA5BMP8fOSRlJEdNQZ/8fD5I= Authentication-Results-Original: dkim=none (message not signed) header.d=none;dmarc=none action=none header.from=arm.com; Received: from VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) by DB9PR08MB9443.eurprd08.prod.outlook.com (2603:10a6:10:45b::19) with Microsoft SMTP Server (version=TLS1_2, cipher=TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384) id 15.20.9009.13; Thu, 7 Aug 2025 16:27:23 +0000 Received: from VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74]) by VI0PR08MB11200.eurprd08.prod.outlook.com ([fe80::d594:64a:dfc:db74%5]) with mapi id 15.20.9009.016; Thu, 7 Aug 2025 16:27:23 +0000 From: Karunika Choo To: dri-devel@lists.freedesktop.org Cc: nd@arm.com, Boris Brezillon , Steven Price , Liviu Dudau , Maarten Lankhorst , Maxime Ripard , Thomas Zimmermann , David Airlie , Simona Vetter , linux-kernel@vger.kernel.org Subject: [PATCH v9 7/7] drm/panthor: Add support for Mali-Gx20 and Mali-Gx25 GPUs Date: Thu, 7 Aug 2025 17:26:33 +0100 Message-ID: <20250807162633.3666310-8-karunika.choo@arm.com> X-Mailer: git-send-email 2.49.0 In-Reply-To: <20250807162633.3666310-1-karunika.choo@arm.com> References: <20250807162633.3666310-1-karunika.choo@arm.com> Content-Transfer-Encoding: quoted-printable X-ClientProxiedBy: LO4P123CA0129.GBRP123.PROD.OUTLOOK.COM (2603:10a6:600:193::8) To VI0PR08MB11200.eurprd08.prod.outlook.com (2603:10a6:800:257::18) Precedence: bulk X-Mailing-List: linux-kernel@vger.kernel.org List-Id: List-Subscribe: List-Unsubscribe: MIME-Version: 1.0 X-MS-TrafficTypeDiagnostic: VI0PR08MB11200:EE_|DB9PR08MB9443:EE_|AM3PEPF0000A78E:EE_|DU0PR08MB9201:EE_ X-MS-Office365-Filtering-Correlation-Id: fe910b80-ffcb-4032-2a01-08ddd5cf5d8c X-LD-Processed: f34e5979-57d9-4aaa-ad4d-b122a662184d,ExtAddr,ExtAddr x-checkrecipientrouted: true NoDisclaimer: true X-MS-Exchange-SenderADCheck: 1 X-MS-Exchange-AntiSpam-Relay: 0 X-Microsoft-Antispam-Untrusted: BCL:0;ARA:13230040|376014|366016|1800799024; X-Microsoft-Antispam-Message-Info-Original: =?us-ascii?Q?LT9HTqCo1mYs3Y8aA/pGYHtcutU4j52oED0i3f2AeBIAbEQTxEFJE5jHQQwd?= =?us-ascii?Q?UlyXtt92to4jptYcCE8VRaVdxG348i/FTNPwLHtfZ3auaG8nIcpLHUFNCsVh?= =?us-ascii?Q?JSqd80vRZA8yVaLtTpLQ60pQ3T2HJpafNNcpZrRpJ9LfiT+C4zeqzVwwsXXQ?= =?us-ascii?Q?fd8ZuyrZV6D/T+pHPxXOXG2ivT6yg1AJPXlXmGdlNU02VbIQZQxREexDL1QE?= =?us-ascii?Q?IwrtS4exCX6/TBLOYby6AXHK1xJJB6/QXerI4TBxs0ngWy6MahtG0txaZHgP?= =?us-ascii?Q?u9QseVS3tOQWK7P2UmPAkYJinI1BptHaEdwKl00iF7kRbkkPlaAfD6A0Nfo4?= =?us-ascii?Q?AcYERQx6aY+HBfTcfmrhuPOwDfjLbwGhJeouVuReZYYFWlfZUynfPjY4qDC5?= =?us-ascii?Q?yWMz3ipdIIok4oQ8Oh+/wx/BS3dkGwHJl9zr1b9B1MtOym2GenO/lawwBAvK?= =?us-ascii?Q?IiVLMoizJY6Ed7Ox9dzf+Lrf+xq51Z6bogrIweGtNHzF/atnjupC51kZuIsz?= =?us-ascii?Q?ILU1qVuP59e1qx4BfNqXleEP94UUfJmm+XL6XCKuFeb2jdrI/uqHC3zHH9f+?= =?us-ascii?Q?aIDrF1Jx73CvRcpyV1GNsAKIlYoAcrwx2h74KOfNR5lWEi/zdwl4+3qvNLtN?= =?us-ascii?Q?jTvAj+YcNm7mWK+xxRin/5wPiRh9UrA4H8eIjPrOq1bLMRXeQZRiRXrUq5ug?= =?us-ascii?Q?dcMvGFS/INaTPA/cyghvFq45CxZtTEJ86HxotfFhdzDdJRhhfKYd0bE1Tpa3?= =?us-ascii?Q?9/IjdsuRGnwhvF/8H/1nOc5xWuaHGg0bA9da6YIsEbwa69Abtn8AzIT/pRnA?= =?us-ascii?Q?lB3dDI/Sz1ne7jBXwvpL+eYAIfbHtD+aGssC+tyfWCF1OywyQfF46urizCQd?= =?us-ascii?Q?HHUGqq6NvkiX0BOKkg3OQatCVsbf6RsuhcgzhngBuMXuC4t15IsQ3S61mCWi?= =?us-ascii?Q?J7XZWqQHItS03Nwopbs7D+crB5cMD/kjrt1FKNcr6+zVx9JGsAUYZusqRD1T?= =?us-ascii?Q?mwthJa9jufeA5FNs6pFf4YFdx5Q+TkpryJAKXyHglcBcJ5d41MR6Jdh4r9oM?= =?us-ascii?Q?Qpwj2bMbCKXgLXUx7m/c9fHjU0LpNHeLuzZPGXBCUKPkdnNexVc0LZpOcjvv?= =?us-ascii?Q?WWEJJxiHJcFaOmN2eIeNAdVo1scYDbWdwDiq9Gv2YMaX+kwP7s89MOwFKzux?= =?us-ascii?Q?yIJJEz2XhBGs0BvQK3VLC1h1dyzSC1fID2060FAKcowWa3uwqybr3zIQum6B?= =?us-ascii?Q?LmwT1Z9EvBm28WlaIk36RBomoWU9xNrV7u88BcMyMbTChkR2UGkch4wpfAXW?= =?us-ascii?Q?qTup/Aj5+HhI5oyA9gxVxbD0HNOZ8OkFTNOVg7jHPw9ZeN2ZXbGY63tuzvDk?= =?us-ascii?Q?wutbeEId7Rd4uTdTsiBscLsbCIkWPMAvNvv14uUk7MYEdrIbVkfJ9hOqBF8b?= =?us-ascii?Q?mZkytuTLBl4=3D?= X-Forefront-Antispam-Report-Untrusted: CIP:255.255.255.255;CTRY:;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:VI0PR08MB11200.eurprd08.prod.outlook.com;PTR:;CAT:NONE;SFS:(13230040)(376014)(366016)(1800799024);DIR:OUT;SFP:1101; X-MS-Exchange-Transport-CrossTenantHeadersStamped: DB9PR08MB9443 X-EOPAttributedMessage: 0 X-MS-Exchange-Transport-CrossTenantHeadersStripped: AM3PEPF0000A78E.eurprd04.prod.outlook.com X-MS-PublicTrafficType: Email X-MS-Office365-Filtering-Correlation-Id-Prvs: fb8cfa2c-9e64-4f7b-b949-08ddd5cf4a38 X-Microsoft-Antispam: BCL:0;ARA:13230040|1800799024|35042699022|376014|82310400026|36860700013|14060799003; X-Microsoft-Antispam-Message-Info: =?us-ascii?Q?yB1v4R9dvQoQtFJ1don8WLfL5J9B9aaAQYyfmhhWQxqVFBU/kPJnDY3sFUhb?= =?us-ascii?Q?7aTSK7JR3h5e6dnblodgMnuNsa775OH0mvGrTTIkXXXBBopcIhK7LJDZB06x?= =?us-ascii?Q?ZWFO/fQVRgbQTNk7NbVkCywWj949xhWJaBR10zYQvNvmqE0u60QlIQn/Jd8u?= =?us-ascii?Q?S/hcR7GYV5SlLwyyQpUQ7kcGdaZa9f/4bD60xJCCpMTzw/O+6F9t5e36kXb4?= =?us-ascii?Q?2OCc7o/k2CKgZleMuFYzPIdU7PAf62uSAURJEtdimbeTBSy/gtlEIo3yqbeS?= =?us-ascii?Q?6BcYre6mSoBV6uhs4t9KYrLg55jQkBm1Wz5PjBtXmJJbp70FqL8/fFxkWx+R?= =?us-ascii?Q?j9Hd9sSY8m0OiugdVptGfIEiOrKf+pD6edEnaJvAQMNmNvc4OqZhF5MKIkNB?= =?us-ascii?Q?eqo4ORSCiKWOMd6GUvyi1IkLE6jIQQDuQxdQnQO+ggRTMN5mgqtlBJfiyO2+?= =?us-ascii?Q?f/ZwyhfEM/Pi+EVGd6TtXNkVnxVtthjxKY3fKvNKCGmM8jArj/ErfHYIsgyI?= =?us-ascii?Q?hm8nQaO+RoZVmqdBt3iL3o1u1SLyt+lhVjD4pLQC863kiQGZIRI3BI3umVz6?= =?us-ascii?Q?sH30b/CYWr/t9eWGWFOQG02CKKj11Yx+SBZ8vQyBGqdn4emZ3T1ZAh824/Jf?= =?us-ascii?Q?DFGbBSYtSdSCsyF52k1U5VeoLB7D5/vr5UKJQwiDozwbZzLwA8GvHsGH4gCX?= =?us-ascii?Q?GPt0iPHhFIKIrEM+U9+s+G6DSDuhaYOMU7AlJ8LBqHSeZZ7MCa4zLheRD38e?= =?us-ascii?Q?8rbGMhDaeq4vARN67D8sXuCjZCuM8sD6Wn0EGrZSQgk9dRT8jsXYGSx0xnv1?= =?us-ascii?Q?j80QrE5BLcrtTIRjvsrbhk/tAjvsIMrhAAWuf8VBshhEFeLPod69ghQbOzmD?= =?us-ascii?Q?/kUnYSdFGLJrENM7vEr+RakHSNvdBPGOohjSrD/pBWmUnlp2gCPs+ljK5yiV?= =?us-ascii?Q?6cgq/DWBPzBs/sY9l+8OFkNW09AWWmRQFcnKpFU5xrOh/rdKOp9hUsX9FU36?= =?us-ascii?Q?6wJU+eLRl8oxpyNK7f9IjHSwdGkQ0fx5x/szp2Fez2pYHf7BER2Yaa2Obqpn?= =?us-ascii?Q?E2yqrBVY2g9k61Y2IayVd8+0hgP7n4e1oSngxyxN/0Rrqg9B/f/GxSNl2Gwb?= =?us-ascii?Q?c4yidCvzKLQarOV3tIbyWfvsnTjV089K5FKh0+1cNlJiVBnHhIY1rWFSqoID?= =?us-ascii?Q?rxhy5BHeWXEV0YwJII4SX6DwRpmGL4mpUdJX18JONLKJhsZS5Tp9xl+KpyAu?= =?us-ascii?Q?+C4JB3yeeIyv6NTVLN0TEwwEkVEAM+0IbBv/frY4ew/YT7FdIqSA2mtIMeTv?= =?us-ascii?Q?XXgzO6jZd0AwuJc+30d0TT0LduCPK8Ts9HxTkS1CYaEHSLA6HgSF8hu+8z0q?= =?us-ascii?Q?ylqDA1+qyNSWi93Pj9cKIJrMg68PVrvdyuA3humyn2+Gb6idm9GRFxaBRxtg?= =?us-ascii?Q?XxTZdNdzFqsH0YXFC5pLnuJ5UhNx3UUzI3UI2J3QZBYIIFQbIF1tNS/wlK6q?= =?us-ascii?Q?ErIyEVX+62ypsEQG7COp5SqdlYwp+lLNWIT9?= X-Forefront-Antispam-Report: CIP:4.158.2.129;CTRY:GB;LANG:en;SCL:1;SRV:;IPV:NLI;SFV:NSPM;H:outbound-uk1.az.dlp.m.darktrace.com;PTR:InfoDomainNonexistent;CAT:NONE;SFS:(13230040)(1800799024)(35042699022)(376014)(82310400026)(36860700013)(14060799003);DIR:OUT;SFP:1101; X-OriginatorOrg: arm.com X-MS-Exchange-CrossTenant-OriginalArrivalTime: 07 Aug 2025 16:27:55.9972 (UTC) X-MS-Exchange-CrossTenant-Network-Message-Id: fe910b80-ffcb-4032-2a01-08ddd5cf5d8c X-MS-Exchange-CrossTenant-Id: f34e5979-57d9-4aaa-ad4d-b122a662184d X-MS-Exchange-CrossTenant-OriginalAttributedTenantConnectingIp: TenantId=f34e5979-57d9-4aaa-ad4d-b122a662184d;Ip=[4.158.2.129];Helo=[outbound-uk1.az.dlp.m.darktrace.com] X-MS-Exchange-CrossTenant-AuthSource: AM3PEPF0000A78E.eurprd04.prod.outlook.com X-MS-Exchange-CrossTenant-AuthAs: Anonymous X-MS-Exchange-CrossTenant-FromEntityHeader: HybridOnPrem X-MS-Exchange-Transport-CrossTenantHeadersStamped: DU0PR08MB9201 Content-Type: text/plain; charset="utf-8" This patch adds firmware binary and GPU model naming support for Mali-Gx20 and Mali-Gx25 GPUs. Reviewed-by: Steven Price Reviewed-by: Liviu Dudau Signed-off-by: Karunika Choo --- drivers/gpu/drm/panthor/panthor_fw.c | 2 ++ drivers/gpu/drm/panthor/panthor_hw.c | 18 ++++++++++++++++++ 2 files changed, 20 insertions(+) diff --git a/drivers/gpu/drm/panthor/panthor_fw.c b/drivers/gpu/drm/panthor= /panthor_fw.c index fa6e0b48a0b2..9bf06e55eaee 100644 --- a/drivers/gpu/drm/panthor/panthor_fw.c +++ b/drivers/gpu/drm/panthor/panthor_fw.c @@ -1405,3 +1405,5 @@ MODULE_FIRMWARE("arm/mali/arch10.8/mali_csffw.bin"); MODULE_FIRMWARE("arm/mali/arch10.10/mali_csffw.bin"); MODULE_FIRMWARE("arm/mali/arch10.12/mali_csffw.bin"); MODULE_FIRMWARE("arm/mali/arch11.8/mali_csffw.bin"); +MODULE_FIRMWARE("arm/mali/arch12.8/mali_csffw.bin"); +MODULE_FIRMWARE("arm/mali/arch13.8/mali_csffw.bin"); diff --git a/drivers/gpu/drm/panthor/panthor_hw.c b/drivers/gpu/drm/panthor= /panthor_hw.c index 8c041e1074a1..4f2858114e5e 100644 --- a/drivers/gpu/drm/panthor/panthor_hw.c +++ b/drivers/gpu/drm/panthor/panthor_hw.c @@ -35,6 +35,24 @@ static char *get_gpu_model_name(struct panthor_device *p= tdev) fallthrough; case GPU_PROD_ID_MAKE(11, 3): return "Mali-G615"; + case GPU_PROD_ID_MAKE(12, 0): + if (shader_core_count >=3D 10 && ray_intersection) + return "Mali-G720-Immortalis"; + else if (shader_core_count >=3D 6) + return "Mali-G720"; + + fallthrough; + case GPU_PROD_ID_MAKE(12, 1): + return "Mali-G620"; + case GPU_PROD_ID_MAKE(13, 0): + if (shader_core_count >=3D 10 && ray_intersection) + return "Mali-G925-Immortalis"; + else if (shader_core_count >=3D 6) + return "Mali-G725"; + + fallthrough; + case GPU_PROD_ID_MAKE(13, 1): + return "Mali-G625"; } =20 return "(Unknown Mali GPU)"; --=20 2.49.0