From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from mga07.intel.com (mga07.intel.com [134.134.136.100]) by gabe.freedesktop.org (Postfix) with ESMTPS id 1683E10E551 for ; Thu, 1 Jun 2023 13:19:18 +0000 (UTC) From: Ville Syrjala To: igt-dev@lists.freedesktop.org Date: Thu, 1 Jun 2023 16:08:50 +0300 Message-Id: <20230601130850.26359-8-ville.syrjala@linux.intel.com> In-Reply-To: <20230601130850.26359-1-ville.syrjala@linux.intel.com> References: <20230601130850.26359-1-ville.syrjala@linux.intel.com> MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit Subject: [igt-dev] [PATCH i-g-t v2 7/7] tests/kms_tiled_display: Override the EDID to fake some tiles List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: igt-dev-bounces@lists.freedesktop.org Sender: "igt-dev" List-ID: From: Ville Syrjälä Pretend we have a tiled display if we don't actually have one. We don't actually know whether the kernel will sync up the displays, but let's assume it does. Signed-off-by: Ville Syrjälä --- tests/kms_tiled_display.c | 128 +++++++++++++++++++++++++++++++++++++- 1 file changed, 126 insertions(+), 2 deletions(-) diff --git a/tests/kms_tiled_display.c b/tests/kms_tiled_display.c index 7f579bacb3d5..d9baf98786a4 100644 --- a/tests/kms_tiled_display.c +++ b/tests/kms_tiled_display.c @@ -111,8 +111,8 @@ static void get_number_of_h_tiles(data_t *data) for (int i = 0; !data->num_h_tiles && i < res->count_connectors; i++) { drmModeConnectorPtr connector; - connector = drmModeGetConnectorCurrent(data->drm_fd, - res->connectors[i]); + connector = drmModeGetConnector(data->drm_fd, + res->connectors[i]); igt_assert(connector); if (connector->connection == DRM_MODE_CONNECTED) { @@ -427,6 +427,119 @@ static void test_with_chamelium(data_t *data) } #endif +static void edid_fill_tile_block(struct edid_ext *ext, + int tile, int num_tiles, + int hdisplay, int vdisplay) +{ + struct dispid_header *dispid; + void *ptr; + + dispid = ptr = edid_ext_dispid(ext); + + ptr = dispid_init(ptr); + ptr = dispid_block_tiled(ptr, num_tiles, 1, + tile, 0, + hdisplay, vdisplay, + "IGT-TILES"); + ptr = dispid_done(dispid, ptr); +} + +static struct edid * +edid_with_tile(const struct edid *old_edid, + const drmModeModeInfo *mode, + int tile, int num_tiles) +{ + struct edid *edid = malloc(edid_get_size(old_edid) + EDID_BLOCK_SIZE); + + memcpy(edid, old_edid, edid_get_size(old_edid)); + edid->extensions_len++; + + edid_fill_tile_block((struct edid_ext *)&edid[edid->extensions_len], + tile, num_tiles, mode->hdisplay, mode->vdisplay); + + edid_update_checksum(edid); + + return edid; +} + +static void force_edid_with_tile(data_t *data, + igt_output_t *output, + const drmModeModeInfo *mode, + int tile, int num_tiles) +{ + struct edid *edid; + drmModePropertyBlobPtr blob; + uint64_t blob_id; + + kmstest_get_property(data->drm_fd, output->id, + DRM_MODE_OBJECT_CONNECTOR, "EDID", + NULL, &blob_id, NULL); + + blob = drmModeGetPropertyBlob(data->drm_fd, blob_id); + edid = edid_with_tile(blob->data, mode, tile, num_tiles); + drmModeFreePropertyBlob(blob); + + kmstest_force_edid(data->drm_fd, output->config.connector, edid); + + free(edid); +} + +static bool mode_equal(const drmModeModeInfo *a, + const drmModeModeInfo *b) +{ + return a->hdisplay == b->hdisplay && + a->hsync_start == b->hsync_start && + a->hsync_end == b->hsync_end && + a->htotal == b->htotal && + a->vdisplay == b->vdisplay && + a->vsync_start == b->vsync_start && + a->vsync_end == b->vsync_end && + a->vtotal == b->vtotal && + a->clock == b->clock && + a->flags == b->flags && + a->hskew == b->hskew && + a->vscan == b->vscan; +} + +static void override_edid(data_t *data) +{ + drmModeModeInfo common_mode = {}; + igt_output_t *outputs[8] = {}; + igt_output_t *output; + int num_outputs = 0; + int num_tiles = 0; + drmModeResPtr res; + + igt_require(data->display.n_pipes >= 2); + + for_each_connected_output(&data->display, output) { + drmModeModeInfo *mode = igt_output_get_mode(output); + + if (!common_mode.hdisplay) + common_mode = *mode; + + if (mode_equal(&common_mode, mode)) { + outputs[num_outputs] = output; + if (++num_outputs >= ARRAY_SIZE(outputs)) + break; + } + } + + igt_require(num_outputs >= 2); + + num_tiles = min(num_outputs, data->display.n_pipes); + + /* disable everything so that we are sure to get a full modeset */ + res = drmModeGetResources(data->drm_fd); + igt_require(res); + kmstest_unset_all_crtcs(data->drm_fd, res); + drmModeFreeResources(res); + + for (int i = 0; i < num_tiles; i++) + force_edid_with_tile(data, outputs[i], + &common_mode, i, num_tiles); +} + static void basic_test(data_t *data, drmEventContext *drm_event, struct pollfd *pfd) { int ret; @@ -470,6 +583,17 @@ igt_main drm_event.page_flip_handler2 = page_flip_handler; data.commit = data.display.is_atomic ? COMMIT_ATOMIC : COMMIT_LEGACY; igt_require(data.commit == COMMIT_ATOMIC); + + get_number_of_h_tiles(&data); + igt_debug("Number of real horizontal tiles: %d\n", data.num_h_tiles); + + if (data.num_h_tiles == 0) { + override_edid(&data); + get_number_of_h_tiles(&data); + + igt_debug("Number of fake horizontal tiles: %d\n", data.num_h_tiles); + } + igt_require(data.num_h_tiles > 0); } igt_describe("Make sure the Tiled CRTCs are synchronized and we get " -- 2.39.3